ViewVC Help

View File | Revision Log | Show Annotations | Download File

/cvs/libev/ev.c

Comparing libev/ev.c (file contents):
Revision 1.456 by root, Thu Jul 4 22:32:23 2013 UTC vs.
Revision 1.500 by root, Mon Jul 1 20:47:37 2019 UTC

1	/*	1	/*
2	* libev event processing core, watcher management	2	* libev event processing core, watcher management
3	*	3	*
4	* Copyright (c) 2007,2008,2009,2010,2011,2012 Marc Alexander Lehmann <libev@schmorp.de>	4	* Copyright (c) 2007-2019 Marc Alexander Lehmann <libev@schmorp.de>
5	* All rights reserved.	5	* All rights reserved.
6	*	6	*
7	* Redistribution and use in source and binary forms, with or without modifica-	7	* Redistribution and use in source and binary forms, with or without modifica-
8	* tion, are permitted provided that the following conditions are met:	8	* tion, are permitted provided that the following conditions are met:
9	*	9	*
…		…
43	# include EV_CONFIG_H	43	# include EV_CONFIG_H
44	# else	44	# else
45	# include "config.h"	45	# include "config.h"
46	# endif	46	# endif
47		47
48	#if HAVE_FLOOR	48	# if HAVE_FLOOR
49	# ifndef EV_USE_FLOOR	49	# ifndef EV_USE_FLOOR
50	# define EV_USE_FLOOR 1	50	# define EV_USE_FLOOR 1
		51	# endif
51	# endif	52	# endif
52	#endif
53		53
54	# if HAVE_CLOCK_SYSCALL	54	# if HAVE_CLOCK_SYSCALL
55	# ifndef EV_USE_CLOCK_SYSCALL	55	# ifndef EV_USE_CLOCK_SYSCALL
56	# define EV_USE_CLOCK_SYSCALL 1	56	# define EV_USE_CLOCK_SYSCALL 1
57	# ifndef EV_USE_REALTIME	57	# ifndef EV_USE_REALTIME
…		…
113	# define EV_USE_EPOLL EV_FEATURE_BACKENDS	113	# define EV_USE_EPOLL EV_FEATURE_BACKENDS
114	# endif	114	# endif
115	# else	115	# else
116	# undef EV_USE_EPOLL	116	# undef EV_USE_EPOLL
117	# define EV_USE_EPOLL 0	117	# define EV_USE_EPOLL 0
		118	# endif
		119
		120	# if HAVE_LINUX_AIO_ABI_H
		121	# ifndef EV_USE_LINUXAIO
		122	# define EV_USE_LINUXAIO EV_FEATURE_BACKENDS
		123	# endif
		124	# else
		125	# undef EV_USE_LINUXAIO
		126	# define EV_USE_LINUXAIO 0
118	# endif	127	# endif
119		128
120	# if HAVE_KQUEUE && HAVE_SYS_EVENT_H	129	# if HAVE_KQUEUE && HAVE_SYS_EVENT_H
121	# ifndef EV_USE_KQUEUE	130	# ifndef EV_USE_KQUEUE
122	# define EV_USE_KQUEUE EV_FEATURE_BACKENDS	131	# define EV_USE_KQUEUE EV_FEATURE_BACKENDS
…		…
162	# define EV_USE_EVENTFD 0	171	# define EV_USE_EVENTFD 0
163	# endif	172	# endif
164		173
165	#endif	174	#endif
166		175
		176	/* OS X, in its infinite idiocy, actually HARDCODES
		177	* a limit of 1024 into their select. Where people have brains,
		178	* OS X engineers apparently have a vacuum. Or maybe they were
		179	* ordered to have a vacuum, or they do anything for money.
		180	* This might help. Or not.
		181	* Note that this must be defined early, as other include files
		182	* will rely on this define as well.
		183	*/
		184	#define _DARWIN_UNLIMITED_SELECT 1
		185
167	#include <stdlib.h>	186	#include <stdlib.h>
168	#include <string.h>	187	#include <string.h>
169	#include <fcntl.h>	188	#include <fcntl.h>
170	#include <stddef.h>	189	#include <stddef.h>
171		190
…		…
208	# ifndef EV_SELECT_IS_WINSOCKET	227	# ifndef EV_SELECT_IS_WINSOCKET
209	# define EV_SELECT_IS_WINSOCKET 1	228	# define EV_SELECT_IS_WINSOCKET 1
210	# endif	229	# endif
211	# undef EV_AVOID_STDIO	230	# undef EV_AVOID_STDIO
212	#endif	231	#endif
213
214	/* OS X, in its infinite idiocy, actually HARDCODES
215	* a limit of 1024 into their select. Where people have brains,
216	* OS X engineers apparently have a vacuum. Or maybe they were
217	* ordered to have a vacuum, or they do anything for money.
218	* This might help. Or not.
219	*/
220	#define _DARWIN_UNLIMITED_SELECT 1
221		232
222	/* this block tries to deduce configuration from header-defined symbols and defaults */	233	/* this block tries to deduce configuration from header-defined symbols and defaults */
223		234
224	/* try to deduce the maximum number of signals on this platform */	235	/* try to deduce the maximum number of signals on this platform */
225	#if defined EV_NSIG	236	#if defined EV_NSIG
…		…
241	#elif defined SIGARRAYSIZE	252	#elif defined SIGARRAYSIZE
242	# define EV_NSIG (SIGARRAYSIZE) /* Assume ary[SIGARRAYSIZE] */	253	# define EV_NSIG (SIGARRAYSIZE) /* Assume ary[SIGARRAYSIZE] */
243	#elif defined _sys_nsig	254	#elif defined _sys_nsig
244	# define EV_NSIG (_sys_nsig) /* Solaris 2.5 */	255	# define EV_NSIG (_sys_nsig) /* Solaris 2.5 */
245	#else	256	#else
246	# error "unable to find value for NSIG, please report"	257	# define EV_NSIG (8 * sizeof (sigset_t) + 1)
247	/* to make it compile regardless, just remove the above line, */
248	/* but consider reporting it, too! :) */
249	# define EV_NSIG 65
250	#endif	258	#endif
251		259
252	#ifndef EV_USE_FLOOR	260	#ifndef EV_USE_FLOOR
253	# define EV_USE_FLOOR 0	261	# define EV_USE_FLOOR 0
254	#endif	262	#endif
255		263
256	#ifndef EV_USE_CLOCK_SYSCALL	264	#ifndef EV_USE_CLOCK_SYSCALL
257	# if __linux && __GLIBC__ >= 2	265	# if __linux && __GLIBC__ == 2 && __GLIBC_MINOR__ < 17
258	# define EV_USE_CLOCK_SYSCALL EV_FEATURE_OS	266	# define EV_USE_CLOCK_SYSCALL EV_FEATURE_OS
259	# else	267	# else
260	# define EV_USE_CLOCK_SYSCALL 0	268	# define EV_USE_CLOCK_SYSCALL 0
		269	# endif
		270	#endif
		271
		272	#if !(_POSIX_TIMERS > 0)
		273	# ifndef EV_USE_MONOTONIC
		274	# define EV_USE_MONOTONIC 0
		275	# endif
		276	# ifndef EV_USE_REALTIME
		277	# define EV_USE_REALTIME 0
261	# endif	278	# endif
262	#endif	279	#endif
263		280
264	#ifndef EV_USE_MONOTONIC	281	#ifndef EV_USE_MONOTONIC
265	# if defined _POSIX_MONOTONIC_CLOCK && _POSIX_MONOTONIC_CLOCK >= 0	282	# if defined _POSIX_MONOTONIC_CLOCK && _POSIX_MONOTONIC_CLOCK >= 0
…		…
307		324
308	#ifndef EV_USE_PORT	325	#ifndef EV_USE_PORT
309	# define EV_USE_PORT 0	326	# define EV_USE_PORT 0
310	#endif	327	#endif
311		328
		329	#ifndef EV_USE_LINUXAIO
		330	# if __linux /* libev currently assumes linux/aio_abi.h is always available on linux */
		331	# define EV_USE_LINUXAIO 1
		332	# else
		333	# define EV_USE_LINUXAIO 0
		334	# endif
		335	#endif
		336
312	#ifndef EV_USE_INOTIFY	337	#ifndef EV_USE_INOTIFY
313	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))	338	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))
314	# define EV_USE_INOTIFY EV_FEATURE_OS	339	# define EV_USE_INOTIFY EV_FEATURE_OS
315	# else	340	# else
316	# define EV_USE_INOTIFY 0	341	# define EV_USE_INOTIFY 0
…		…
357		382
358	#ifndef EV_HEAP_CACHE_AT	383	#ifndef EV_HEAP_CACHE_AT
359	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA	384	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA
360	#endif	385	#endif
361		386
362	#ifdef ANDROID	387	#ifdef __ANDROID__
363	/* supposedly, android doesn't typedef fd_mask */	388	/* supposedly, android doesn't typedef fd_mask */
364	# undef EV_USE_SELECT	389	# undef EV_USE_SELECT
365	# define EV_USE_SELECT 0	390	# define EV_USE_SELECT 0
366	/* supposedly, we need to include syscall.h, not sys/syscall.h, so just disable */	391	/* supposedly, we need to include syscall.h, not sys/syscall.h, so just disable */
367	# undef EV_USE_CLOCK_SYSCALL	392	# undef EV_USE_CLOCK_SYSCALL
…		…
408		433
409	#if !EV_USE_NANOSLEEP	434	#if !EV_USE_NANOSLEEP
410	/* hp-ux has it in sys/time.h, which we unconditionally include above */	435	/* hp-ux has it in sys/time.h, which we unconditionally include above */
411	# if !defined _WIN32 && !defined __hpux	436	# if !defined _WIN32 && !defined __hpux
412	# include <sys/select.h>	437	# include <sys/select.h>
		438	# endif
		439	#endif
		440
		441	#if EV_USE_LINUXAIO
		442	# include <sys/syscall.h>
		443	# if !SYS_io_getevents || !EV_USE_EPOLL /* ev_linxaio uses ev_poll.c:ev_epoll_create */
		444	# undef EV_USE_LINUXAIO
		445	# define EV_USE_LINUXAIO 0
413	# endif	446	# endif
414	#endif	447	#endif
415		448
416	#if EV_USE_INOTIFY	449	#if EV_USE_INOTIFY
417	# include <sys/statfs.h>	450	# include <sys/statfs.h>
…		…
485	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */	518	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */
486	/* ECB.H BEGIN */	519	/* ECB.H BEGIN */
487	/*	520	/*
488	* libecb - http://software.schmorp.de/pkg/libecb	521	* libecb - http://software.schmorp.de/pkg/libecb
489	*	522	*
490	* Copyright (©) 2009-2012 Marc Alexander Lehmann <libecb@schmorp.de>	523	* Copyright (©) 2009-2015 Marc Alexander Lehmann <libecb@schmorp.de>
491	* Copyright (©) 2011 Emanuele Giaquinta	524	* Copyright (©) 2011 Emanuele Giaquinta
492	* All rights reserved.	525	* All rights reserved.
493	*	526	*
494	* Redistribution and use in source and binary forms, with or without modifica-	527	* Redistribution and use in source and binary forms, with or without modifica-
495	* tion, are permitted provided that the following conditions are met:	528	* tion, are permitted provided that the following conditions are met:
…		…
509	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;	542	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;
510	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,	543	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,
511	* WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING NEGLIGENCE OR OTH-	544	* WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING NEGLIGENCE OR OTH-
512	* ERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED	545	* ERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED
513	* OF THE POSSIBILITY OF SUCH DAMAGE.	546	* OF THE POSSIBILITY OF SUCH DAMAGE.
		547	*
		548	* Alternatively, the contents of this file may be used under the terms of
		549	* the GNU General Public License ("GPL") version 2 or any later version,
		550	* in which case the provisions of the GPL are applicable instead of
		551	* the above. If you wish to allow the use of your version of this file
		552	* only under the terms of the GPL and not to allow others to use your
		553	* version of this file under the BSD license, indicate your decision
		554	* by deleting the provisions above and replace them with the notice
		555	* and other provisions required by the GPL. If you do not delete the
		556	* provisions above, a recipient may use your version of this file under
		557	* either the BSD or the GPL.
514	*/	558	*/
515		559
516	#ifndef ECB_H	560	#ifndef ECB_H
517	#define ECB_H	561	#define ECB_H
518		562
519	/* 16 bits major, 16 bits minor */	563	/* 16 bits major, 16 bits minor */
520	#define ECB_VERSION 0x00010003	564	#define ECB_VERSION 0x00010006
521		565
522	#ifdef _WIN32	566	#ifdef _WIN32
523	typedef signed char int8_t;	567	typedef signed char int8_t;
524	typedef unsigned char uint8_t;	568	typedef unsigned char uint8_t;
525	typedef signed short int16_t;	569	typedef signed short int16_t;
…		…
542	typedef uint32_t uintptr_t;	586	typedef uint32_t uintptr_t;
543	typedef int32_t intptr_t;	587	typedef int32_t intptr_t;
544	#endif	588	#endif
545	#else	589	#else
546	#include <inttypes.h>	590	#include <inttypes.h>
547	#if UINTMAX_MAX > 0xffffffffU	591	#if (defined INTPTR_MAX ? INTPTR_MAX : ULONG_MAX) > 0xffffffffU
548	#define ECB_PTRSIZE 8	592	#define ECB_PTRSIZE 8
549	#else	593	#else
550	#define ECB_PTRSIZE 4	594	#define ECB_PTRSIZE 4
551	#endif	595	#endif
552	#endif	596	#endif
553		597
		598	#define ECB_GCC_AMD64 (__amd64 || __amd64__ || __x86_64 || __x86_64__)
		599	#define ECB_MSVC_AMD64 (_M_AMD64 || _M_X64)
		600
554	/* work around x32 idiocy by defining proper macros */	601	/* work around x32 idiocy by defining proper macros */
555	#if __x86_64 || _M_AMD64	602	#if ECB_GCC_AMD64 || ECB_MSVC_AMD64
556	#if __ILP32	603	#if _ILP32
557	#define ECB_AMD64_X32 1	604	#define ECB_AMD64_X32 1
558	#else	605	#else
559	#define ECB_AMD64 1	606	#define ECB_AMD64 1
560	#endif	607	#endif
561	#endif	608	#endif
…		…
565	* causing enormous grief in return for some better fake benchmark numbers.	612	* causing enormous grief in return for some better fake benchmark numbers.
566	* or so.	613	* or so.
567	* we try to detect these and simply assume they are not gcc - if they have	614	* we try to detect these and simply assume they are not gcc - if they have
568	* an issue with that they should have done it right in the first place.	615	* an issue with that they should have done it right in the first place.
569	*/	616	*/
570	#ifndef ECB_GCC_VERSION
571	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__	617	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__
572	#define ECB_GCC_VERSION(major,minor) 0	618	#define ECB_GCC_VERSION(major,minor) 0
573	#else	619	#else
574	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))	620	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))
575	#endif	621	#endif
576	#endif
577		622
578	#define ECB_C (__STDC__+0) /* this assumes that __STDC__ is either empty or a number */	623	#define ECB_CLANG_VERSION(major,minor) (__clang_major__ > (major) || (__clang_major__ == (major) && __clang_minor__ >= (minor)))
579	#define ECB_C99 (__STDC_VERSION__ >= 199901L)	624
580	#define ECB_C11 (__STDC_VERSION__ >= 201112L)	625	#if __clang__ && defined __has_builtin
		626	#define ECB_CLANG_BUILTIN(x) __has_builtin (x)
		627	#else
		628	#define ECB_CLANG_BUILTIN(x) 0
		629	#endif
		630
		631	#if __clang__ && defined __has_extension
		632	#define ECB_CLANG_EXTENSION(x) __has_extension (x)
		633	#else
		634	#define ECB_CLANG_EXTENSION(x) 0
		635	#endif
		636
581	#define ECB_CPP (__cplusplus+0)	637	#define ECB_CPP (__cplusplus+0)
582	#define ECB_CPP11 (__cplusplus >= 201103L)	638	#define ECB_CPP11 (__cplusplus >= 201103L)
		639	#define ECB_CPP14 (__cplusplus >= 201402L)
		640	#define ECB_CPP17 (__cplusplus >= 201703L)
		641
		642	#if ECB_CPP
		643	#define ECB_C 0
		644	#define ECB_STDC_VERSION 0
		645	#else
		646	#define ECB_C 1
		647	#define ECB_STDC_VERSION __STDC_VERSION__
		648	#endif
		649
		650	#define ECB_C99 (ECB_STDC_VERSION >= 199901L)
		651	#define ECB_C11 (ECB_STDC_VERSION >= 201112L)
		652	#define ECB_C17 (ECB_STDC_VERSION >= 201710L)
583		653
584	#if ECB_CPP	654	#if ECB_CPP
585	#define ECB_EXTERN_C extern "C"	655	#define ECB_EXTERN_C extern "C"
586	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {	656	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {
587	#define ECB_EXTERN_C_END }	657	#define ECB_EXTERN_C_END }
…		…
602		672
603	#if ECB_NO_SMP	673	#if ECB_NO_SMP
604	#define ECB_MEMORY_FENCE do { } while (0)	674	#define ECB_MEMORY_FENCE do { } while (0)
605	#endif	675	#endif
606		676
		677	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/compiler_ref/compiler_builtins.html */
		678	#if __xlC__ && ECB_CPP
		679	#include <builtins.h>
		680	#endif
		681
		682	#if 1400 <= _MSC_VER
		683	#include <intrin.h> /* fence functions _ReadBarrier, also bit search functions _BitScanReverse */
		684	#endif
		685
607	#ifndef ECB_MEMORY_FENCE	686	#ifndef ECB_MEMORY_FENCE
608	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	687	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
		688	#define ECB_MEMORY_FENCE_RELAXED __asm__ __volatile__ ("" : : : "memory")
609	#if __i386 || __i386__	689	#if __i386 || __i386__
610	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")	690	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")
611	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")	691	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
612	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	692	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
613	#elif __amd64 || __amd64__ || __x86_64 || __x86_64__	693	#elif ECB_GCC_AMD64
614	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")	694	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")
615	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")	695	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
616	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	696	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
617	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__	697	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__
618	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")	698	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")
		699	#elif defined __ARM_ARCH_2__ \
		700	|| defined __ARM_ARCH_3__ || defined __ARM_ARCH_3M__ \
		701	|| defined __ARM_ARCH_4__ || defined __ARM_ARCH_4T__ \
		702	|| defined __ARM_ARCH_5__ || defined __ARM_ARCH_5E__ \
		703	|| defined __ARM_ARCH_5T__ || defined __ARM_ARCH_5TE__ \
		704	|| defined __ARM_ARCH_5TEJ__
		705	/* should not need any, unless running old code on newer cpu - arm doesn't support that */
619	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \	706	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \
620	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__	707	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__ \
		708	|| defined __ARM_ARCH_6T2__
621	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")	709	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")
622	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \	710	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \
623	|| defined __ARM_ARCH_7M__ || defined __ARM_ARCH_7R__	711	|| defined __ARM_ARCH_7R__ || defined __ARM_ARCH_7M__
624	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")	712	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")
625	#elif __sparc || __sparc__	713	#elif __aarch64__
		714	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb ish" : : : "memory")
		715	#elif (__sparc || __sparc__) && !(__sparc_v8__ || defined __sparcv8)
626	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")	716	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")
627	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")	717	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")
628	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")	718	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")
629	#elif defined __s390__ || defined __s390x__	719	#elif defined __s390__ || defined __s390x__
630	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")	720	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")
631	#elif defined __mips__	721	#elif defined __mips__
632	/* GNU/Linux emulates sync on mips1 architectures, so we force it's use */	722	/* GNU/Linux emulates sync on mips1 architectures, so we force its use */
633	/* anybody else who still uses mips1 is supposed to send in their version, with detection code. */	723	/* anybody else who still uses mips1 is supposed to send in their version, with detection code. */
634	#define ECB_MEMORY_FENCE __asm__ __volatile__ (".set mips2; sync; .set mips0" : : : "memory")	724	#define ECB_MEMORY_FENCE __asm__ __volatile__ (".set mips2; sync; .set mips0" : : : "memory")
635	#elif defined __alpha__	725	#elif defined __alpha__
636	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mb" : : : "memory")	726	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mb" : : : "memory")
637	#elif defined __hppa__	727	#elif defined __hppa__
638	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("" : : : "memory")	728	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("" : : : "memory")
639	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	729	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")
640	#elif defined __ia64__	730	#elif defined __ia64__
641	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mf" : : : "memory")	731	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mf" : : : "memory")
		732	#elif defined __m68k__
		733	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("" : : : "memory")
		734	#elif defined __m88k__
		735	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("tb1 0,%%r0,128" : : : "memory")
		736	#elif defined __sh__
		737	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("" : : : "memory")
642	#endif	738	#endif
643	#endif	739	#endif
644	#endif	740	#endif
645		741
646	#ifndef ECB_MEMORY_FENCE	742	#ifndef ECB_MEMORY_FENCE
647	#if ECB_GCC_VERSION(4,7)	743	#if ECB_GCC_VERSION(4,7)
648	/* see comment below (stdatomic.h) about the C11 memory model. */	744	/* see comment below (stdatomic.h) about the C11 memory model. */
649	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)	745	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)
		746	#define ECB_MEMORY_FENCE_ACQUIRE __atomic_thread_fence (__ATOMIC_ACQUIRE)
		747	#define ECB_MEMORY_FENCE_RELEASE __atomic_thread_fence (__ATOMIC_RELEASE)
		748	#define ECB_MEMORY_FENCE_RELAXED __atomic_thread_fence (__ATOMIC_RELAXED)
650		749
651	/* The __has_feature syntax from clang is so misdesigned that we cannot use it	750	#elif ECB_CLANG_EXTENSION(c_atomic)
652	* without risking compile time errors with other compilers. We *could*
653	* define our own ecb_clang_has_feature, but I just can't be bothered to work
654	* around this shit time and again.
655	* #elif defined __clang && __has_feature (cxx_atomic)
656	* // see comment below (stdatomic.h) about the C11 memory model.	751	/* see comment below (stdatomic.h) about the C11 memory model. */
657	* #define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)	752	#define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)
658	*/	753	#define ECB_MEMORY_FENCE_ACQUIRE __c11_atomic_thread_fence (__ATOMIC_ACQUIRE)
		754	#define ECB_MEMORY_FENCE_RELEASE __c11_atomic_thread_fence (__ATOMIC_RELEASE)
		755	#define ECB_MEMORY_FENCE_RELAXED __c11_atomic_thread_fence (__ATOMIC_RELAXED)
659		756
660	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__	757	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__
661	#define ECB_MEMORY_FENCE __sync_synchronize ()	758	#define ECB_MEMORY_FENCE __sync_synchronize ()
		759	#elif _MSC_VER >= 1500 /* VC++ 2008 */
		760	/* apparently, microsoft broke all the memory barrier stuff in Visual Studio 2008... */
		761	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)
		762	#define ECB_MEMORY_FENCE _ReadWriteBarrier (); MemoryBarrier()
		763	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier (); MemoryBarrier() /* according to msdn, _ReadBarrier is not a load fence */
		764	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier (); MemoryBarrier()
662	#elif _MSC_VER >= 1400 /* VC++ 2005 */	765	#elif _MSC_VER >= 1400 /* VC++ 2005 */
663	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)	766	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)
664	#define ECB_MEMORY_FENCE _ReadWriteBarrier ()	767	#define ECB_MEMORY_FENCE _ReadWriteBarrier ()
665	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier () /* according to msdn, _ReadBarrier is not a load fence */	768	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier () /* according to msdn, _ReadBarrier is not a load fence */
666	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier ()	769	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier ()
667	#elif defined _WIN32	770	#elif defined _WIN32
668	#include <WinNT.h>	771	#include <WinNT.h>
669	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */	772	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */
670	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	773	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
671	#include <mbarrier.h>	774	#include <mbarrier.h>
672	#define ECB_MEMORY_FENCE __machine_rw_barrier ()	775	#define ECB_MEMORY_FENCE __machine_rw_barrier ()
673	#define ECB_MEMORY_FENCE_ACQUIRE __machine_r_barrier ()	776	#define ECB_MEMORY_FENCE_ACQUIRE __machine_acq_barrier ()
674	#define ECB_MEMORY_FENCE_RELEASE __machine_w_barrier ()	777	#define ECB_MEMORY_FENCE_RELEASE __machine_rel_barrier ()
		778	#define ECB_MEMORY_FENCE_RELAXED __compiler_barrier ()
675	#elif __xlC__	779	#elif __xlC__
676	#define ECB_MEMORY_FENCE __sync ()	780	#define ECB_MEMORY_FENCE __sync ()
677	#endif	781	#endif
678	#endif	782	#endif
679		783
680	#ifndef ECB_MEMORY_FENCE	784	#ifndef ECB_MEMORY_FENCE
681	#if ECB_C11 && !defined __STDC_NO_ATOMICS__	785	#if ECB_C11 && !defined __STDC_NO_ATOMICS__
682	/* we assume that these memory fences work on all variables/all memory accesses, */	786	/* we assume that these memory fences work on all variables/all memory accesses, */
683	/* not just C11 atomics and atomic accesses */	787	/* not just C11 atomics and atomic accesses */
684	#include <stdatomic.h>	788	#include <stdatomic.h>
685	/* Unfortunately, neither gcc 4.7 nor clang 3.1 generate any instructions for */
686	/* any fence other than seq_cst, which isn't very efficient for us. */
687	/* Why that is, we don't know - either the C11 memory model is quite useless */
688	/* for most usages, or gcc and clang have a bug */
689	/* I *currently* lean towards the latter, and inefficiently implement */
690	/* all three of ecb's fences as a seq_cst fence */
691	#define ECB_MEMORY_FENCE atomic_thread_fence (memory_order_seq_cst)	789	#define ECB_MEMORY_FENCE atomic_thread_fence (memory_order_seq_cst)
		790	#define ECB_MEMORY_FENCE_ACQUIRE atomic_thread_fence (memory_order_acquire)
		791	#define ECB_MEMORY_FENCE_RELEASE atomic_thread_fence (memory_order_release)
692	#endif	792	#endif
693	#endif	793	#endif
694		794
695	#ifndef ECB_MEMORY_FENCE	795	#ifndef ECB_MEMORY_FENCE
696	#if !ECB_AVOID_PTHREADS	796	#if !ECB_AVOID_PTHREADS
…		…
716		816
717	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE	817	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE
718	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	818	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
719	#endif	819	#endif
720		820
		821	#if !defined ECB_MEMORY_FENCE_RELAXED && defined ECB_MEMORY_FENCE
		822	#define ECB_MEMORY_FENCE_RELAXED ECB_MEMORY_FENCE /* very heavy-handed */
		823	#endif
		824
721	/*****************************************************************************/	825	/*****************************************************************************/
722		826
723	#if __cplusplus	827	#if ECB_CPP
724	#define ecb_inline static inline	828	#define ecb_inline static inline
725	#elif ECB_GCC_VERSION(2,5)	829	#elif ECB_GCC_VERSION(2,5)
726	#define ecb_inline static __inline__	830	#define ecb_inline static __inline__
727	#elif ECB_C99	831	#elif ECB_C99
728	#define ecb_inline static inline	832	#define ecb_inline static inline
…		…
742		846
743	#define ECB_CONCAT_(a, b) a ## b	847	#define ECB_CONCAT_(a, b) a ## b
744	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)	848	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)
745	#define ECB_STRINGIFY_(a) # a	849	#define ECB_STRINGIFY_(a) # a
746	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)	850	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)
		851	#define ECB_STRINGIFY_EXPR(expr) ((expr), ECB_STRINGIFY_ (expr))
747		852
748	#define ecb_function_ ecb_inline	853	#define ecb_function_ ecb_inline
749		854
750	#if ECB_GCC_VERSION(3,1)	855	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_VERSION(2,8)
751	#define ecb_attribute(attrlist) __attribute__(attrlist)	856	#define ecb_attribute(attrlist) __attribute__ (attrlist)
		857	#else
		858	#define ecb_attribute(attrlist)
		859	#endif
		860
		861	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_constant_p)
752	#define ecb_is_constant(expr) __builtin_constant_p (expr)	862	#define ecb_is_constant(expr) __builtin_constant_p (expr)
		863	#else
		864	/* possible C11 impl for integral types
		865	typedef struct ecb_is_constant_struct ecb_is_constant_struct;
		866	#define ecb_is_constant(expr) _Generic ((1 ? (struct ecb_is_constant_struct *)0 : (void *)((expr) - (expr)), ecb_is_constant_struct *: 0, default: 1)) */
		867
		868	#define ecb_is_constant(expr) 0
		869	#endif
		870
		871	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_expect)
753	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))	872	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))
		873	#else
		874	#define ecb_expect(expr,value) (expr)
		875	#endif
		876
		877	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_prefetch)
754	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)	878	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)
755	#else	879	#else
756	#define ecb_attribute(attrlist)
757	#define ecb_is_constant(expr) 0
758	#define ecb_expect(expr,value) (expr)
759	#define ecb_prefetch(addr,rw,locality)	880	#define ecb_prefetch(addr,rw,locality)
760	#endif	881	#endif
761		882
762	/* no emulation for ecb_decltype */	883	/* no emulation for ecb_decltype */
763	#if ECB_GCC_VERSION(4,5)	884	#if ECB_CPP11
		885	// older implementations might have problems with decltype(x)::type, work around it
		886	template<class T> struct ecb_decltype_t { typedef T type; };
764	#define ecb_decltype(x) __decltype(x)	887	#define ecb_decltype(x) ecb_decltype_t<decltype (x)>::type
765	#elif ECB_GCC_VERSION(3,0)	888	#elif ECB_GCC_VERSION(3,0) || ECB_CLANG_VERSION(2,8)
766	#define ecb_decltype(x) __typeof(x)	889	#define ecb_decltype(x) __typeof__ (x)
767	#endif	890	#endif
768		891
		892	#if _MSC_VER >= 1300
		893	#define ecb_deprecated __declspec (deprecated)
		894	#else
		895	#define ecb_deprecated ecb_attribute ((__deprecated__))
		896	#endif
		897
		898	#if _MSC_VER >= 1500
		899	#define ecb_deprecated_message(msg) __declspec (deprecated (msg))
		900	#elif ECB_GCC_VERSION(4,5)
		901	#define ecb_deprecated_message(msg) ecb_attribute ((__deprecated__ (msg))
		902	#else
		903	#define ecb_deprecated_message(msg) ecb_deprecated
		904	#endif
		905
		906	#if _MSC_VER >= 1400
		907	#define ecb_noinline __declspec (noinline)
		908	#else
769	#define ecb_noinline ecb_attribute ((__noinline__))	909	#define ecb_noinline ecb_attribute ((__noinline__))
		910	#endif
		911
770	#define ecb_unused ecb_attribute ((__unused__))	912	#define ecb_unused ecb_attribute ((__unused__))
771	#define ecb_const ecb_attribute ((__const__))	913	#define ecb_const ecb_attribute ((__const__))
772	#define ecb_pure ecb_attribute ((__pure__))	914	#define ecb_pure ecb_attribute ((__pure__))
773		915
774	#if ECB_C11	916	#if ECB_C11 || __IBMC_NORETURN
		917	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/language_ref/noreturn.html */
775	#define ecb_noreturn _Noreturn	918	#define ecb_noreturn _Noreturn
		919	#elif ECB_CPP11
		920	#define ecb_noreturn [[noreturn]]
		921	#elif _MSC_VER >= 1200
		922	/* http://msdn.microsoft.com/en-us/library/k6ktzx3s.aspx */
		923	#define ecb_noreturn __declspec (noreturn)
776	#else	924	#else
777	#define ecb_noreturn ecb_attribute ((__noreturn__))	925	#define ecb_noreturn ecb_attribute ((__noreturn__))
778	#endif	926	#endif
779		927
780	#if ECB_GCC_VERSION(4,3)	928	#if ECB_GCC_VERSION(4,3)
…		…
795	/* for compatibility to the rest of the world */	943	/* for compatibility to the rest of the world */
796	#define ecb_likely(expr) ecb_expect_true (expr)	944	#define ecb_likely(expr) ecb_expect_true (expr)
797	#define ecb_unlikely(expr) ecb_expect_false (expr)	945	#define ecb_unlikely(expr) ecb_expect_false (expr)
798		946
799	/* count trailing zero bits and count # of one bits */	947	/* count trailing zero bits and count # of one bits */
800	#if ECB_GCC_VERSION(3,4)	948	#if ECB_GCC_VERSION(3,4) \
		949	|| (ECB_CLANG_BUILTIN(__builtin_clz) && ECB_CLANG_BUILTIN(__builtin_clzll) \
		950	&& ECB_CLANG_BUILTIN(__builtin_ctz) && ECB_CLANG_BUILTIN(__builtin_ctzll) \
		951	&& ECB_CLANG_BUILTIN(__builtin_popcount))
801	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */	952	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */
802	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)	953	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)
803	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)	954	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)
804	#define ecb_ctz32(x) __builtin_ctz (x)	955	#define ecb_ctz32(x) __builtin_ctz (x)
805	#define ecb_ctz64(x) __builtin_ctzll (x)	956	#define ecb_ctz64(x) __builtin_ctzll (x)
806	#define ecb_popcount32(x) __builtin_popcount (x)	957	#define ecb_popcount32(x) __builtin_popcount (x)
807	/* no popcountll */	958	/* no popcountll */
808	#else	959	#else
809	ecb_function_ int ecb_ctz32 (uint32_t x) ecb_const;	960	ecb_function_ ecb_const int ecb_ctz32 (uint32_t x);
810	ecb_function_ int	961	ecb_function_ ecb_const int
811	ecb_ctz32 (uint32_t x)	962	ecb_ctz32 (uint32_t x)
812	{	963	{
		964	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		965	unsigned long r;
		966	_BitScanForward (&r, x);
		967	return (int)r;
		968	#else
813	int r = 0;	969	int r = 0;
814		970
815	x &= ~x + 1; /* this isolates the lowest bit */	971	x &= ~x + 1; /* this isolates the lowest bit */
816		972
817	#if ECB_branchless_on_i386	973	#if ECB_branchless_on_i386
…		…
827	if (x & 0xff00ff00) r += 8;	983	if (x & 0xff00ff00) r += 8;
828	if (x & 0xffff0000) r += 16;	984	if (x & 0xffff0000) r += 16;
829	#endif	985	#endif
830		986
831	return r;	987	return r;
		988	#endif
832	}	989	}
833		990
834	ecb_function_ int ecb_ctz64 (uint64_t x) ecb_const;	991	ecb_function_ ecb_const int ecb_ctz64 (uint64_t x);
835	ecb_function_ int	992	ecb_function_ ecb_const int
836	ecb_ctz64 (uint64_t x)	993	ecb_ctz64 (uint64_t x)
837	{	994	{
		995	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		996	unsigned long r;
		997	_BitScanForward64 (&r, x);
		998	return (int)r;
		999	#else
838	int shift = x & 0xffffffffU ? 0 : 32;	1000	int shift = x & 0xffffffff ? 0 : 32;
839	return ecb_ctz32 (x >> shift) + shift;	1001	return ecb_ctz32 (x >> shift) + shift;
		1002	#endif
840	}	1003	}
841		1004
842	ecb_function_ int ecb_popcount32 (uint32_t x) ecb_const;	1005	ecb_function_ ecb_const int ecb_popcount32 (uint32_t x);
843	ecb_function_ int	1006	ecb_function_ ecb_const int
844	ecb_popcount32 (uint32_t x)	1007	ecb_popcount32 (uint32_t x)
845	{	1008	{
846	x -= (x >> 1) & 0x55555555;	1009	x -= (x >> 1) & 0x55555555;
847	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);	1010	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);
848	x = ((x >> 4) + x) & 0x0f0f0f0f;	1011	x = ((x >> 4) + x) & 0x0f0f0f0f;
849	x *= 0x01010101;	1012	x *= 0x01010101;
850		1013
851	return x >> 24;	1014	return x >> 24;
852	}	1015	}
853		1016
854	ecb_function_ int ecb_ld32 (uint32_t x) ecb_const;	1017	ecb_function_ ecb_const int ecb_ld32 (uint32_t x);
855	ecb_function_ int ecb_ld32 (uint32_t x)	1018	ecb_function_ ecb_const int ecb_ld32 (uint32_t x)
856	{	1019	{
		1020	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		1021	unsigned long r;
		1022	_BitScanReverse (&r, x);
		1023	return (int)r;
		1024	#else
857	int r = 0;	1025	int r = 0;
858		1026
859	if (x >> 16) { x >>= 16; r += 16; }	1027	if (x >> 16) { x >>= 16; r += 16; }
860	if (x >> 8) { x >>= 8; r += 8; }	1028	if (x >> 8) { x >>= 8; r += 8; }
861	if (x >> 4) { x >>= 4; r += 4; }	1029	if (x >> 4) { x >>= 4; r += 4; }
862	if (x >> 2) { x >>= 2; r += 2; }	1030	if (x >> 2) { x >>= 2; r += 2; }
863	if (x >> 1) { r += 1; }	1031	if (x >> 1) { r += 1; }
864		1032
865	return r;	1033	return r;
		1034	#endif
866	}	1035	}
867		1036
868	ecb_function_ int ecb_ld64 (uint64_t x) ecb_const;	1037	ecb_function_ ecb_const int ecb_ld64 (uint64_t x);
869	ecb_function_ int ecb_ld64 (uint64_t x)	1038	ecb_function_ ecb_const int ecb_ld64 (uint64_t x)
870	{	1039	{
		1040	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1041	unsigned long r;
		1042	_BitScanReverse64 (&r, x);
		1043	return (int)r;
		1044	#else
871	int r = 0;	1045	int r = 0;
872		1046
873	if (x >> 32) { x >>= 32; r += 32; }	1047	if (x >> 32) { x >>= 32; r += 32; }
874		1048
875	return r + ecb_ld32 (x);	1049	return r + ecb_ld32 (x);
		1050	#endif
876	}	1051	}
877	#endif	1052	#endif
878		1053
879	ecb_function_ ecb_bool ecb_is_pot32 (uint32_t x) ecb_const;	1054	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x);
880	ecb_function_ ecb_bool ecb_is_pot32 (uint32_t x) { return !(x & (x - 1)); }	1055	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x) { return !(x & (x - 1)); }
881	ecb_function_ ecb_bool ecb_is_pot64 (uint64_t x) ecb_const;	1056	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x);
882	ecb_function_ ecb_bool ecb_is_pot64 (uint64_t x) { return !(x & (x - 1)); }	1057	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x) { return !(x & (x - 1)); }
883		1058
884	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x) ecb_const;	1059	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x);
885	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x)	1060	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x)
886	{	1061	{
887	return ( (x * 0x0802U & 0x22110U)	1062	return ( (x * 0x0802U & 0x22110U)
888	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;	1063	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;
889	}	1064	}
890		1065
891	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x) ecb_const;	1066	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x);
892	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x)	1067	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x)
893	{	1068	{
894	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);	1069	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);
895	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);	1070	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);
896	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);	1071	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);
897	x = ( x >> 8 ) | ( x << 8);	1072	x = ( x >> 8 ) | ( x << 8);
898		1073
899	return x;	1074	return x;
900	}	1075	}
901		1076
902	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x) ecb_const;	1077	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x);
903	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x)	1078	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x)
904	{	1079	{
905	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);	1080	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);
906	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);	1081	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);
907	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);	1082	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);
908	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);	1083	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);
…		…
911	return x;	1086	return x;
912	}	1087	}
913		1088
914	/* popcount64 is only available on 64 bit cpus as gcc builtin */	1089	/* popcount64 is only available on 64 bit cpus as gcc builtin */
915	/* so for this version we are lazy */	1090	/* so for this version we are lazy */
916	ecb_function_ int ecb_popcount64 (uint64_t x) ecb_const;	1091	ecb_function_ ecb_const int ecb_popcount64 (uint64_t x);
917	ecb_function_ int	1092	ecb_function_ ecb_const int
918	ecb_popcount64 (uint64_t x)	1093	ecb_popcount64 (uint64_t x)
919	{	1094	{
920	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);	1095	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);
921	}	1096	}
922		1097
923	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) ecb_const;	1098	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count);
924	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) ecb_const;	1099	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count);
925	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) ecb_const;	1100	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count);
926	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) ecb_const;	1101	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count);
927	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) ecb_const;	1102	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count);
928	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) ecb_const;	1103	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count);
929	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) ecb_const;	1104	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count);
930	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) ecb_const;	1105	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count);
931		1106
932	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }	1107	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }
933	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }	1108	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }
934	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }	1109	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }
935	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }	1110	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }
936	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }	1111	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }
937	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }	1112	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }
938	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }	1113	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }
939	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }	1114	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }
940		1115
941	#if ECB_GCC_VERSION(4,3)	1116	#if ECB_GCC_VERSION(4,3) || (ECB_CLANG_BUILTIN(__builtin_bswap32) && ECB_CLANG_BUILTIN(__builtin_bswap64))
		1117	#if ECB_GCC_VERSION(4,8) || ECB_CLANG_BUILTIN(__builtin_bswap16)
		1118	#define ecb_bswap16(x) __builtin_bswap16 (x)
		1119	#else
942	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)	1120	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)
		1121	#endif
943	#define ecb_bswap32(x) __builtin_bswap32 (x)	1122	#define ecb_bswap32(x) __builtin_bswap32 (x)
944	#define ecb_bswap64(x) __builtin_bswap64 (x)	1123	#define ecb_bswap64(x) __builtin_bswap64 (x)
		1124	#elif _MSC_VER
		1125	#include <stdlib.h>
		1126	#define ecb_bswap16(x) ((uint16_t)_byteswap_ushort ((uint16_t)(x)))
		1127	#define ecb_bswap32(x) ((uint32_t)_byteswap_ulong ((uint32_t)(x)))
		1128	#define ecb_bswap64(x) ((uint64_t)_byteswap_uint64 ((uint64_t)(x)))
945	#else	1129	#else
946	ecb_function_ uint16_t ecb_bswap16 (uint16_t x) ecb_const;	1130	ecb_function_ ecb_const uint16_t ecb_bswap16 (uint16_t x);
947	ecb_function_ uint16_t	1131	ecb_function_ ecb_const uint16_t
948	ecb_bswap16 (uint16_t x)	1132	ecb_bswap16 (uint16_t x)
949	{	1133	{
950	return ecb_rotl16 (x, 8);	1134	return ecb_rotl16 (x, 8);
951	}	1135	}
952		1136
953	ecb_function_ uint32_t ecb_bswap32 (uint32_t x) ecb_const;	1137	ecb_function_ ecb_const uint32_t ecb_bswap32 (uint32_t x);
954	ecb_function_ uint32_t	1138	ecb_function_ ecb_const uint32_t
955	ecb_bswap32 (uint32_t x)	1139	ecb_bswap32 (uint32_t x)
956	{	1140	{
957	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);	1141	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);
958	}	1142	}
959		1143
960	ecb_function_ uint64_t ecb_bswap64 (uint64_t x) ecb_const;	1144	ecb_function_ ecb_const uint64_t ecb_bswap64 (uint64_t x);
961	ecb_function_ uint64_t	1145	ecb_function_ ecb_const uint64_t
962	ecb_bswap64 (uint64_t x)	1146	ecb_bswap64 (uint64_t x)
963	{	1147	{
964	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);	1148	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);
965	}	1149	}
966	#endif	1150	#endif
967		1151
968	#if ECB_GCC_VERSION(4,5)	1152	#if ECB_GCC_VERSION(4,5) || ECB_CLANG_BUILTIN(__builtin_unreachable)
969	#define ecb_unreachable() __builtin_unreachable ()	1153	#define ecb_unreachable() __builtin_unreachable ()
970	#else	1154	#else
971	/* this seems to work fine, but gcc always emits a warning for it :/ */	1155	/* this seems to work fine, but gcc always emits a warning for it :/ */
972	ecb_inline void ecb_unreachable (void) ecb_noreturn;	1156	ecb_inline ecb_noreturn void ecb_unreachable (void);
973	ecb_inline void ecb_unreachable (void) { }	1157	ecb_inline ecb_noreturn void ecb_unreachable (void) { }
974	#endif	1158	#endif
975		1159
976	/* try to tell the compiler that some condition is definitely true */	1160	/* try to tell the compiler that some condition is definitely true */
977	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0	1161	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0
978		1162
979	ecb_inline unsigned char ecb_byteorder_helper (void) ecb_const;	1163	ecb_inline ecb_const uint32_t ecb_byteorder_helper (void);
980	ecb_inline unsigned char	1164	ecb_inline ecb_const uint32_t
981	ecb_byteorder_helper (void)	1165	ecb_byteorder_helper (void)
982	{	1166	{
983	/* the union code still generates code under pressure in gcc, */	1167	/* the union code still generates code under pressure in gcc, */
984	/* but less than using pointers, and always seems to */	1168	/* but less than using pointers, and always seems to */
985	/* successfully return a constant. */	1169	/* successfully return a constant. */
986	/* the reason why we have this horrible preprocessor mess */	1170	/* the reason why we have this horrible preprocessor mess */
987	/* is to avoid it in all cases, at least on common architectures */	1171	/* is to avoid it in all cases, at least on common architectures */
988	/* or when using a recent enough gcc version (>= 4.6) */	1172	/* or when using a recent enough gcc version (>= 4.6) */
989	#if __i386 || __i386__ || _M_X86 || __amd64 || __amd64__ || _M_X64
990	return 0x44;
991	#elif __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_LITTLE_ENDIAN__	1173	#if (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_LITTLE_ENDIAN__) \
		1174	|| ((__i386 || __i386__ || _M_IX86 || ECB_GCC_AMD64 || ECB_MSVC_AMD64) && !__VOS__)
		1175	#define ECB_LITTLE_ENDIAN 1
992	return 0x44;	1176	return 0x44332211;
993	#elif __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__	1177	#elif (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__) \
		1178	|| ((__AARCH64EB__ || __MIPSEB__ || __ARMEB__) && !__VOS__)
		1179	#define ECB_BIG_ENDIAN 1
994	return 0x11;	1180	return 0x11223344;
995	#else	1181	#else
996	union	1182	union
997	{	1183	{
		1184	uint8_t c[4];
998	uint32_t i;	1185	uint32_t u;
999	uint8_t c;
1000	} u = { 0x11223344 };	1186	} u = { 0x11, 0x22, 0x33, 0x44 };
1001	return u.c;	1187	return u.u;
1002	#endif	1188	#endif
1003	}	1189	}
1004		1190
1005	ecb_inline ecb_bool ecb_big_endian (void) ecb_const;	1191	ecb_inline ecb_const ecb_bool ecb_big_endian (void);
1006	ecb_inline ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11; }	1192	ecb_inline ecb_const ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11223344; }
1007	ecb_inline ecb_bool ecb_little_endian (void) ecb_const;	1193	ecb_inline ecb_const ecb_bool ecb_little_endian (void);
1008	ecb_inline ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44; }	1194	ecb_inline ecb_const ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44332211; }
1009		1195
1010	#if ECB_GCC_VERSION(3,0) || ECB_C99	1196	#if ECB_GCC_VERSION(3,0) || ECB_C99
1011	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))	1197	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))
1012	#else	1198	#else
1013	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))	1199	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))
1014	#endif	1200	#endif
1015		1201
1016	#if __cplusplus	1202	#if ECB_CPP
1017	template<typename T>	1203	template<typename T>
1018	static inline T ecb_div_rd (T val, T div)	1204	static inline T ecb_div_rd (T val, T div)
1019	{	1205	{
1020	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;	1206	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;
1021	}	1207	}
…		…
1038	}	1224	}
1039	#else	1225	#else
1040	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))	1226	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))
1041	#endif	1227	#endif
1042		1228
		1229	ecb_function_ ecb_const uint32_t ecb_binary16_to_binary32 (uint32_t x);
		1230	ecb_function_ ecb_const uint32_t
		1231	ecb_binary16_to_binary32 (uint32_t x)
		1232	{
		1233	unsigned int s = (x & 0x8000) << (31 - 15);
		1234	int e = (x >> 10) & 0x001f;
		1235	unsigned int m = x & 0x03ff;
		1236
		1237	if (ecb_expect_false (e == 31))
		1238	/* infinity or NaN */
		1239	e = 255 - (127 - 15);
		1240	else if (ecb_expect_false (!e))
		1241	{
		1242	if (ecb_expect_true (!m))
		1243	/* zero, handled by code below by forcing e to 0 */
		1244	e = 0 - (127 - 15);
		1245	else
		1246	{
		1247	/* subnormal, renormalise */
		1248	unsigned int s = 10 - ecb_ld32 (m);
		1249
		1250	m = (m << s) & 0x3ff; /* mask implicit bit */
		1251	e -= s - 1;
		1252	}
		1253	}
		1254
		1255	/* e and m now are normalised, or zero, (or inf or nan) */
		1256	e += 127 - 15;
		1257
		1258	return s | (e << 23) | (m << (23 - 10));
		1259	}
		1260
		1261	ecb_function_ ecb_const uint16_t ecb_binary32_to_binary16 (uint32_t x);
		1262	ecb_function_ ecb_const uint16_t
		1263	ecb_binary32_to_binary16 (uint32_t x)
		1264	{
		1265	unsigned int s = (x >> 16) & 0x00008000; /* sign bit, the easy part */
		1266	unsigned int e = ((x >> 23) & 0x000000ff) - (127 - 15); /* the desired exponent */
		1267	unsigned int m = x & 0x007fffff;
		1268
		1269	x &= 0x7fffffff;
		1270
		1271	/* if it's within range of binary16 normals, use fast path */
		1272	if (ecb_expect_true (0x38800000 <= x && x <= 0x477fefff))
		1273	{
		1274	/* mantissa round-to-even */
		1275	m += 0x00000fff + ((m >> (23 - 10)) & 1);
		1276
		1277	/* handle overflow */
		1278	if (ecb_expect_false (m >= 0x00800000))
		1279	{
		1280	m >>= 1;
		1281	e += 1;
		1282	}
		1283
		1284	return s | (e << 10) | (m >> (23 - 10));
		1285	}
		1286
		1287	/* handle large numbers and infinity */
		1288	if (ecb_expect_true (0x477fefff < x && x <= 0x7f800000))
		1289	return s | 0x7c00;
		1290
		1291	/* handle zero, subnormals and small numbers */
		1292	if (ecb_expect_true (x < 0x38800000))
		1293	{
		1294	/* zero */
		1295	if (ecb_expect_true (!x))
		1296	return s;
		1297
		1298	/* handle subnormals */
		1299
		1300	/* too small, will be zero */
		1301	if (e < (14 - 24)) /* might not be sharp, but is good enough */
		1302	return s;
		1303
		1304	m |= 0x00800000; /* make implicit bit explicit */
		1305
		1306	/* very tricky - we need to round to the nearest e (+10) bit value */
		1307	{
		1308	unsigned int bits = 14 - e;
		1309	unsigned int half = (1 << (bits - 1)) - 1;
		1310	unsigned int even = (m >> bits) & 1;
		1311
		1312	/* if this overflows, we will end up with a normalised number */
		1313	m = (m + half + even) >> bits;
		1314	}
		1315
		1316	return s | m;
		1317	}
		1318
		1319	/* handle NaNs, preserve leftmost nan bits, but make sure we don't turn them into infinities */
		1320	m >>= 13;
		1321
		1322	return s | 0x7c00 | m | !m;
		1323	}
		1324
1043	/*******************************************************************************/	1325	/*******************************************************************************/
1044	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */	1326	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */
1045		1327
1046	/* basically, everything uses "ieee pure-endian" floating point numbers */	1328	/* basically, everything uses "ieee pure-endian" floating point numbers */
1047	/* the only noteworthy exception is ancient armle, which uses order 43218765 */	1329	/* the only noteworthy exception is ancient armle, which uses order 43218765 */
1048	#if 0 \	1330	#if 0 \
1049	|| __i386 || __i386__ \	1331	|| __i386 || __i386__ \
1050	|| __amd64 || __amd64__ || __x86_64 || __x86_64__ \	1332	|| ECB_GCC_AMD64 \
1051	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \	1333	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \
1052	|| defined __arm__ && defined __ARM_EABI__ \
1053	|| defined __s390__ || defined __s390x__ \	1334	|| defined __s390__ || defined __s390x__ \
1054	|| defined __mips__ \	1335	|| defined __mips__ \
1055	|| defined __alpha__ \	1336	|| defined __alpha__ \
1056	|| defined __hppa__ \	1337	|| defined __hppa__ \
1057	|| defined __ia64__ \	1338	|| defined __ia64__ \
		1339	|| defined __m68k__ \
		1340	|| defined __m88k__ \
		1341	|| defined __sh__ \
1058	|| defined _M_IX86 || defined _M_AMD64 || defined _M_IA64	1342	|| defined _M_IX86 || defined ECB_MSVC_AMD64 || defined _M_IA64 \
		1343	|| (defined __arm__ && (defined __ARM_EABI__ || defined __EABI__ || defined __VFP_FP__ || defined _WIN32_WCE || defined __ANDROID__)) \
		1344	|| defined __aarch64__
1059	#define ECB_STDFP 1	1345	#define ECB_STDFP 1
1060	#include <string.h> /* for memcpy */	1346	#include <string.h> /* for memcpy */
1061	#else	1347	#else
1062	#define ECB_STDFP 0	1348	#define ECB_STDFP 0
1063	#include <math.h> /* for frexp*, ldexp* */
1064	#endif	1349	#endif
1065		1350
1066	#ifndef ECB_NO_LIBM	1351	#ifndef ECB_NO_LIBM
1067		1352
		1353	#include <math.h> /* for frexp*, ldexp*, INFINITY, NAN */
		1354
		1355	/* only the oldest of old doesn't have this one. solaris. */
		1356	#ifdef INFINITY
		1357	#define ECB_INFINITY INFINITY
		1358	#else
		1359	#define ECB_INFINITY HUGE_VAL
		1360	#endif
		1361
		1362	#ifdef NAN
		1363	#define ECB_NAN NAN
		1364	#else
		1365	#define ECB_NAN ECB_INFINITY
		1366	#endif
		1367
		1368	#if ECB_C99 || _XOPEN_VERSION >= 600 || _POSIX_VERSION >= 200112L
		1369	#define ecb_ldexpf(x,e) ldexpf ((x), (e))
		1370	#define ecb_frexpf(x,e) frexpf ((x), (e))
		1371	#else
		1372	#define ecb_ldexpf(x,e) (float) ldexp ((double) (x), (e))
		1373	#define ecb_frexpf(x,e) (float) frexp ((double) (x), (e))
		1374	#endif
		1375
1068	/* convert a float to ieee single/binary32 */	1376	/* convert a float to ieee single/binary32 */
1069	ecb_function_ uint32_t ecb_float_to_binary32 (float x) ecb_const;	1377	ecb_function_ ecb_const uint32_t ecb_float_to_binary32 (float x);
1070	ecb_function_ uint32_t	1378	ecb_function_ ecb_const uint32_t
1071	ecb_float_to_binary32 (float x)	1379	ecb_float_to_binary32 (float x)
1072	{	1380	{
1073	uint32_t r;	1381	uint32_t r;
1074		1382
1075	#if ECB_STDFP	1383	#if ECB_STDFP
…		…
1082	if (x == 0e0f ) return 0x00000000U;	1390	if (x == 0e0f ) return 0x00000000U;
1083	if (x > +3.40282346638528860e+38f) return 0x7f800000U;	1391	if (x > +3.40282346638528860e+38f) return 0x7f800000U;
1084	if (x < -3.40282346638528860e+38f) return 0xff800000U;	1392	if (x < -3.40282346638528860e+38f) return 0xff800000U;
1085	if (x != x ) return 0x7fbfffffU;	1393	if (x != x ) return 0x7fbfffffU;
1086		1394
1087	m = frexpf (x, &e) * 0x1000000U;	1395	m = ecb_frexpf (x, &e) * 0x1000000U;
1088		1396
1089	r = m & 0x80000000U;	1397	r = m & 0x80000000U;
1090		1398
1091	if (r)	1399	if (r)
1092	m = -m;	1400	m = -m;
…		…
1104		1412
1105	return r;	1413	return r;
1106	}	1414	}
1107		1415
1108	/* converts an ieee single/binary32 to a float */	1416	/* converts an ieee single/binary32 to a float */
1109	ecb_function_ float ecb_binary32_to_float (uint32_t x) ecb_const;	1417	ecb_function_ ecb_const float ecb_binary32_to_float (uint32_t x);
1110	ecb_function_ float	1418	ecb_function_ ecb_const float
1111	ecb_binary32_to_float (uint32_t x)	1419	ecb_binary32_to_float (uint32_t x)
1112	{	1420	{
1113	float r;	1421	float r;
1114		1422
1115	#if ECB_STDFP	1423	#if ECB_STDFP
…		…
1125	x |= 0x800000U;	1433	x |= 0x800000U;
1126	else	1434	else
1127	e = 1;	1435	e = 1;
1128		1436
1129	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */	1437	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */
1130	r = ldexpf (x * (0.5f / 0x800000U), e - 126);	1438	r = ecb_ldexpf (x * (0.5f / 0x800000U), e - 126);
1131		1439
1132	r = neg ? -r : r;	1440	r = neg ? -r : r;
1133	#endif	1441	#endif
1134		1442
1135	return r;	1443	return r;
1136	}	1444	}
1137		1445
1138	/* convert a double to ieee double/binary64 */	1446	/* convert a double to ieee double/binary64 */
1139	ecb_function_ uint64_t ecb_double_to_binary64 (double x) ecb_const;	1447	ecb_function_ ecb_const uint64_t ecb_double_to_binary64 (double x);
1140	ecb_function_ uint64_t	1448	ecb_function_ ecb_const uint64_t
1141	ecb_double_to_binary64 (double x)	1449	ecb_double_to_binary64 (double x)
1142	{	1450	{
1143	uint64_t r;	1451	uint64_t r;
1144		1452
1145	#if ECB_STDFP	1453	#if ECB_STDFP
…		…
1174		1482
1175	return r;	1483	return r;
1176	}	1484	}
1177		1485
1178	/* converts an ieee double/binary64 to a double */	1486	/* converts an ieee double/binary64 to a double */
1179	ecb_function_ double ecb_binary64_to_double (uint64_t x) ecb_const;	1487	ecb_function_ ecb_const double ecb_binary64_to_double (uint64_t x);
1180	ecb_function_ double	1488	ecb_function_ ecb_const double
1181	ecb_binary64_to_double (uint64_t x)	1489	ecb_binary64_to_double (uint64_t x)
1182	{	1490	{
1183	double r;	1491	double r;
1184		1492
1185	#if ECB_STDFP	1493	#if ECB_STDFP
…		…
1203	#endif	1511	#endif
1204		1512
1205	return r;	1513	return r;
1206	}	1514	}
1207		1515
		1516	/* convert a float to ieee half/binary16 */
		1517	ecb_function_ ecb_const uint16_t ecb_float_to_binary16 (float x);
		1518	ecb_function_ ecb_const uint16_t
		1519	ecb_float_to_binary16 (float x)
		1520	{
		1521	return ecb_binary32_to_binary16 (ecb_float_to_binary32 (x));
		1522	}
		1523
		1524	/* convert an ieee half/binary16 to float */
		1525	ecb_function_ ecb_const float ecb_binary16_to_float (uint16_t x);
		1526	ecb_function_ ecb_const float
		1527	ecb_binary16_to_float (uint16_t x)
		1528	{
		1529	return ecb_binary32_to_float (ecb_binary16_to_binary32 (x));
		1530	}
		1531
1208	#endif	1532	#endif
1209		1533
1210	#endif	1534	#endif
1211		1535
1212	/* ECB.H END */	1536	/* ECB.H END */
1213		1537
1214	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS	1538	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS
1215	/* if your architecture doesn't need memory fences, e.g. because it is	1539	/* if your architecture doesn't need memory fences, e.g. because it is
1216	* single-cpu/core, or if you use libev in a project that doesn't use libev	1540	* single-cpu/core, or if you use libev in a project that doesn't use libev
1217	* from multiple threads, then you can define ECB_AVOID_PTHREADS when compiling	1541	* from multiple threads, then you can define ECB_NO_THREADS when compiling
1218	* libev, in which cases the memory fences become nops.	1542	* libev, in which cases the memory fences become nops.
1219	* alternatively, you can remove this #error and link against libpthread,	1543	* alternatively, you can remove this #error and link against libpthread,
1220	* which will then provide the memory fences.	1544	* which will then provide the memory fences.
1221	*/	1545	*/
1222	# error "memory fences not defined for your architecture, please report"	1546	# error "memory fences not defined for your architecture, please report"
…		…
1226	# define ECB_MEMORY_FENCE do { } while (0)	1550	# define ECB_MEMORY_FENCE do { } while (0)
1227	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE	1551	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE
1228	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	1552	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
1229	#endif	1553	#endif
1230		1554
1231	#define expect_false(cond) ecb_expect_false (cond)
1232	#define expect_true(cond) ecb_expect_true (cond)
1233	#define noinline ecb_noinline
1234
1235	#define inline_size ecb_inline	1555	#define inline_size ecb_inline
1236		1556
1237	#if EV_FEATURE_CODE	1557	#if EV_FEATURE_CODE
1238	# define inline_speed ecb_inline	1558	# define inline_speed ecb_inline
1239	#else	1559	#else
1240	# define inline_speed static noinline	1560	# define inline_speed ecb_noinline static
1241	#endif	1561	#endif
1242		1562
1243	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)	1563	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)
1244		1564
1245	#if EV_MINPRI == EV_MAXPRI	1565	#if EV_MINPRI == EV_MAXPRI
1246	# define ABSPRI(w) (((W)w), 0)	1566	# define ABSPRI(w) (((W)w), 0)
1247	#else	1567	#else
1248	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)	1568	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)
1249	#endif	1569	#endif
1250		1570
1251	#define EMPTY /* required for microsofts broken pseudo-c compiler */	1571	#define EMPTY /* required for microsofts broken pseudo-c compiler */
1252	#define EMPTY2(a,b) /* used to suppress some warnings */
1253		1572
1254	typedef ev_watcher *W;	1573	typedef ev_watcher *W;
1255	typedef ev_watcher_list *WL;	1574	typedef ev_watcher_list *WL;
1256	typedef ev_watcher_time *WT;	1575	typedef ev_watcher_time *WT;
1257		1576
…		…
1282	# include "ev_win32.c"	1601	# include "ev_win32.c"
1283	#endif	1602	#endif
1284		1603
1285	/*****************************************************************************/	1604	/*****************************************************************************/
1286		1605
		1606	#if EV_USE_LINUXAIO
		1607	# include <linux/aio_abi.h> /* probably only needed for aio_context_t */
		1608	#endif
		1609
1287	/* define a suitable floor function (only used by periodics atm) */	1610	/* define a suitable floor function (only used by periodics atm) */
1288		1611
1289	#if EV_USE_FLOOR	1612	#if EV_USE_FLOOR
1290	# include <math.h>	1613	# include <math.h>
1291	# define ev_floor(v) floor (v)	1614	# define ev_floor(v) floor (v)
1292	#else	1615	#else
1293		1616
1294	#include <float.h>	1617	#include <float.h>
1295		1618
1296	/* a floor() replacement function, should be independent of ev_tstamp type */	1619	/* a floor() replacement function, should be independent of ev_tstamp type */
		1620	ecb_noinline
1297	static ev_tstamp noinline	1621	static ev_tstamp
1298	ev_floor (ev_tstamp v)	1622	ev_floor (ev_tstamp v)
1299	{	1623	{
1300	/* the choice of shift factor is not terribly important */	1624	/* the choice of shift factor is not terribly important */
1301	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */	1625	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */
1302	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;	1626	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;
1303	#else	1627	#else
1304	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;	1628	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;
1305	#endif	1629	#endif
1306		1630
1307	/* argument too large for an unsigned long? */	1631	/* argument too large for an unsigned long? */
1308	if (expect_false (v >= shift))	1632	if (ecb_expect_false (v >= shift))
1309	{	1633	{
1310	ev_tstamp f;	1634	ev_tstamp f;
1311		1635
1312	if (v == v - 1.)	1636	if (v == v - 1.)
1313	return v; /* very large number */	1637	return v; /* very large number */
…		…
1315	f = shift * ev_floor (v * (1. / shift));	1639	f = shift * ev_floor (v * (1. / shift));
1316	return f + ev_floor (v - f);	1640	return f + ev_floor (v - f);
1317	}	1641	}
1318		1642
1319	/* special treatment for negative args? */	1643	/* special treatment for negative args? */
1320	if (expect_false (v < 0.))	1644	if (ecb_expect_false (v < 0.))
1321	{	1645	{
1322	ev_tstamp f = -ev_floor (-v);	1646	ev_tstamp f = -ev_floor (-v);
1323		1647
1324	return f - (f == v ? 0 : 1);	1648	return f - (f == v ? 0 : 1);
1325	}	1649	}
…		…
1334		1658
1335	#ifdef __linux	1659	#ifdef __linux
1336	# include <sys/utsname.h>	1660	# include <sys/utsname.h>
1337	#endif	1661	#endif
1338		1662
1339	static unsigned int noinline ecb_cold	1663	ecb_noinline ecb_cold
		1664	static unsigned int
1340	ev_linux_version (void)	1665	ev_linux_version (void)
1341	{	1666	{
1342	#ifdef __linux	1667	#ifdef __linux
1343	unsigned int v = 0;	1668	unsigned int v = 0;
1344	struct utsname buf;	1669	struct utsname buf;
…		…
1373	}	1698	}
1374		1699
1375	/*****************************************************************************/	1700	/*****************************************************************************/
1376		1701
1377	#if EV_AVOID_STDIO	1702	#if EV_AVOID_STDIO
1378	static void noinline ecb_cold	1703	ecb_noinline ecb_cold
		1704	static void
1379	ev_printerr (const char *msg)	1705	ev_printerr (const char *msg)
1380	{	1706	{
1381	write (STDERR_FILENO, msg, strlen (msg));	1707	write (STDERR_FILENO, msg, strlen (msg));
1382	}	1708	}
1383	#endif	1709	#endif
1384		1710
1385	static void (*syserr_cb)(const char *msg) EV_THROW;	1711	static void (*syserr_cb)(const char *msg) EV_NOEXCEPT;
1386		1712
1387	void ecb_cold	1713	ecb_cold
		1714	void
1388	ev_set_syserr_cb (void (*cb)(const char *msg) EV_THROW) EV_THROW	1715	ev_set_syserr_cb (void (*cb)(const char *msg) EV_NOEXCEPT) EV_NOEXCEPT
1389	{	1716	{
1390	syserr_cb = cb;	1717	syserr_cb = cb;
1391	}	1718	}
1392		1719
1393	static void noinline ecb_cold	1720	ecb_noinline ecb_cold
		1721	static void
1394	ev_syserr (const char *msg)	1722	ev_syserr (const char *msg)
1395	{	1723	{
1396	if (!msg)	1724	if (!msg)
1397	msg = "(libev) system error";	1725	msg = "(libev) system error";
1398		1726
…		…
1411	abort ();	1739	abort ();
1412	}	1740	}
1413	}	1741	}
1414		1742
1415	static void *	1743	static void *
1416	ev_realloc_emul (void *ptr, long size) EV_THROW	1744	ev_realloc_emul (void *ptr, long size) EV_NOEXCEPT
1417	{	1745	{
1418	/* some systems, notably openbsd and darwin, fail to properly	1746	/* some systems, notably openbsd and darwin, fail to properly
1419	* implement realloc (x, 0) (as required by both ansi c-89 and	1747	* implement realloc (x, 0) (as required by both ansi c-89 and
1420	* the single unix specification, so work around them here.	1748	* the single unix specification, so work around them here.
1421	* recently, also (at least) fedora and debian started breaking it,	1749	* recently, also (at least) fedora and debian started breaking it,
…		…
1427		1755
1428	free (ptr);	1756	free (ptr);
1429	return 0;	1757	return 0;
1430	}	1758	}
1431		1759
1432	static void *(*alloc)(void *ptr, long size) EV_THROW = ev_realloc_emul;	1760	static void *(*alloc)(void *ptr, long size) EV_NOEXCEPT = ev_realloc_emul;
1433		1761
1434	void ecb_cold	1762	ecb_cold
		1763	void
1435	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_THROW) EV_THROW	1764	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_NOEXCEPT) EV_NOEXCEPT
1436	{	1765	{
1437	alloc = cb;	1766	alloc = cb;
1438	}	1767	}
1439		1768
1440	inline_speed void *	1769	inline_speed void *
…		…
1467	typedef struct	1796	typedef struct
1468	{	1797	{
1469	WL head;	1798	WL head;
1470	unsigned char events; /* the events watched for */	1799	unsigned char events; /* the events watched for */
1471	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */	1800	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */
1472	unsigned char emask; /* the epoll backend stores the actual kernel mask in here */	1801	unsigned char emask; /* some backends store the actual kernel mask in here */
1473	unsigned char unused;	1802	unsigned char unused;
1474	#if EV_USE_EPOLL	1803	#if EV_USE_EPOLL
1475	unsigned int egen; /* generation counter to counter epoll bugs */	1804	unsigned int egen; /* generation counter to counter epoll bugs */
1476	#endif	1805	#endif
1477	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP	1806	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP
…		…
1542	static int ev_default_loop_ptr;	1871	static int ev_default_loop_ptr;
1543		1872
1544	#endif	1873	#endif
1545		1874
1546	#if EV_FEATURE_API	1875	#if EV_FEATURE_API
1547	# define EV_RELEASE_CB if (expect_false (release_cb)) release_cb (EV_A)	1876	# define EV_RELEASE_CB if (ecb_expect_false (release_cb)) release_cb (EV_A)
1548	# define EV_ACQUIRE_CB if (expect_false (acquire_cb)) acquire_cb (EV_A)	1877	# define EV_ACQUIRE_CB if (ecb_expect_false (acquire_cb)) acquire_cb (EV_A)
1549	# define EV_INVOKE_PENDING invoke_cb (EV_A)	1878	# define EV_INVOKE_PENDING invoke_cb (EV_A)
1550	#else	1879	#else
1551	# define EV_RELEASE_CB (void)0	1880	# define EV_RELEASE_CB (void)0
1552	# define EV_ACQUIRE_CB (void)0	1881	# define EV_ACQUIRE_CB (void)0
1553	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)	1882	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)
…		…
1557		1886
1558	/*****************************************************************************/	1887	/*****************************************************************************/
1559		1888
1560	#ifndef EV_HAVE_EV_TIME	1889	#ifndef EV_HAVE_EV_TIME
1561	ev_tstamp	1890	ev_tstamp
1562	ev_time (void) EV_THROW	1891	ev_time (void) EV_NOEXCEPT
1563	{	1892	{
1564	#if EV_USE_REALTIME	1893	#if EV_USE_REALTIME
1565	if (expect_true (have_realtime))	1894	if (ecb_expect_true (have_realtime))
1566	{	1895	{
1567	struct timespec ts;	1896	struct timespec ts;
1568	clock_gettime (CLOCK_REALTIME, &ts);	1897	clock_gettime (CLOCK_REALTIME, &ts);
1569	return ts.tv_sec + ts.tv_nsec * 1e-9;	1898	return ts.tv_sec + ts.tv_nsec * 1e-9;
1570	}	1899	}
…		…
1578		1907
1579	inline_size ev_tstamp	1908	inline_size ev_tstamp
1580	get_clock (void)	1909	get_clock (void)
1581	{	1910	{
1582	#if EV_USE_MONOTONIC	1911	#if EV_USE_MONOTONIC
1583	if (expect_true (have_monotonic))	1912	if (ecb_expect_true (have_monotonic))
1584	{	1913	{
1585	struct timespec ts;	1914	struct timespec ts;
1586	clock_gettime (CLOCK_MONOTONIC, &ts);	1915	clock_gettime (CLOCK_MONOTONIC, &ts);
1587	return ts.tv_sec + ts.tv_nsec * 1e-9;	1916	return ts.tv_sec + ts.tv_nsec * 1e-9;
1588	}	1917	}
…		…
1591	return ev_time ();	1920	return ev_time ();
1592	}	1921	}
1593		1922
1594	#if EV_MULTIPLICITY	1923	#if EV_MULTIPLICITY
1595	ev_tstamp	1924	ev_tstamp
1596	ev_now (EV_P) EV_THROW	1925	ev_now (EV_P) EV_NOEXCEPT
1597	{	1926	{
1598	return ev_rt_now;	1927	return ev_rt_now;
1599	}	1928	}
1600	#endif	1929	#endif
1601		1930
1602	void	1931	void
1603	ev_sleep (ev_tstamp delay) EV_THROW	1932	ev_sleep (ev_tstamp delay) EV_NOEXCEPT
1604	{	1933	{
1605	if (delay > 0.)	1934	if (delay > 0.)
1606	{	1935	{
1607	#if EV_USE_NANOSLEEP	1936	#if EV_USE_NANOSLEEP
1608	struct timespec ts;	1937	struct timespec ts;
1609		1938
1610	EV_TS_SET (ts, delay);	1939	EV_TS_SET (ts, delay);
1611	nanosleep (&ts, 0);	1940	nanosleep (&ts, 0);
1612	#elif defined _WIN32	1941	#elif defined _WIN32
		1942	/* maybe this should round up, as ms is very low resolution */
		1943	/* compared to select (µs) or nanosleep (ns) */
1613	Sleep ((unsigned long)(delay * 1e3));	1944	Sleep ((unsigned long)(delay * 1e3));
1614	#else	1945	#else
1615	struct timeval tv;	1946	struct timeval tv;
1616		1947
1617	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */	1948	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */
…		…
1648	}	1979	}
1649		1980
1650	return ncur;	1981	return ncur;
1651	}	1982	}
1652		1983
1653	static void * noinline ecb_cold	1984	ecb_noinline ecb_cold
		1985	static void *
1654	array_realloc (int elem, void *base, int *cur, int cnt)	1986	array_realloc (int elem, void *base, int *cur, int cnt)
1655	{	1987	{
1656	*cur = array_nextsize (elem, *cur, cnt);	1988	*cur = array_nextsize (elem, *cur, cnt);
1657	return ev_realloc (base, elem * *cur);	1989	return ev_realloc (base, elem * *cur);
1658	}	1990	}
1659		1991
		1992	#define array_needsize_noinit(base,offset,count)
		1993
1660	#define array_init_zero(base,count) \	1994	#define array_needsize_zerofill(base,offset,count) \
1661	memset ((void *)(base), 0, sizeof (*(base)) * (count))	1995	memset ((void *)(base + offset), 0, sizeof (*(base)) * (count))
1662		1996
1663	#define array_needsize(type,base,cur,cnt,init) \	1997	#define array_needsize(type,base,cur,cnt,init) \
1664	if (expect_false ((cnt) > (cur))) \	1998	if (ecb_expect_false ((cnt) > (cur))) \
1665	{ \	1999	{ \
1666	int ecb_unused ocur_ = (cur); \	2000	ecb_unused int ocur_ = (cur); \
1667	(base) = (type *)array_realloc \	2001	(base) = (type *)array_realloc \
1668	(sizeof (type), (base), &(cur), (cnt)); \	2002	(sizeof (type), (base), &(cur), (cnt)); \
1669	init ((base) + (ocur_), (cur) - ocur_); \	2003	init ((base), ocur_, ((cur) - ocur_)); \
1670	}	2004	}
1671		2005
1672	#if 0	2006	#if 0
1673	#define array_slim(type,stem) \	2007	#define array_slim(type,stem) \
1674	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \	2008	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \
…		…
1683	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0	2017	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0
1684		2018
1685	/*****************************************************************************/	2019	/*****************************************************************************/
1686		2020
1687	/* dummy callback for pending events */	2021	/* dummy callback for pending events */
1688	static void noinline	2022	ecb_noinline
		2023	static void
1689	pendingcb (EV_P_ ev_prepare *w, int revents)	2024	pendingcb (EV_P_ ev_prepare *w, int revents)
1690	{	2025	{
1691	}	2026	}
1692		2027
1693	void noinline	2028	ecb_noinline
		2029	void
1694	ev_feed_event (EV_P_ void *w, int revents) EV_THROW	2030	ev_feed_event (EV_P_ void *w, int revents) EV_NOEXCEPT
1695	{	2031	{
1696	W w_ = (W)w;	2032	W w_ = (W)w;
1697	int pri = ABSPRI (w_);	2033	int pri = ABSPRI (w_);
1698		2034
1699	if (expect_false (w_->pending))	2035	if (ecb_expect_false (w_->pending))
1700	pendings [pri][w_->pending - 1].events |= revents;	2036	pendings [pri][w_->pending - 1].events |= revents;
1701	else	2037	else
1702	{	2038	{
1703	w_->pending = ++pendingcnt [pri];	2039	w_->pending = ++pendingcnt [pri];
1704	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, EMPTY2);	2040	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, array_needsize_noinit);
1705	pendings [pri][w_->pending - 1].w = w_;	2041	pendings [pri][w_->pending - 1].w = w_;
1706	pendings [pri][w_->pending - 1].events = revents;	2042	pendings [pri][w_->pending - 1].events = revents;
1707	}	2043	}
1708		2044
1709	pendingpri = NUMPRI - 1;	2045	pendingpri = NUMPRI - 1;
1710	}	2046	}
1711		2047
1712	inline_speed void	2048	inline_speed void
1713	feed_reverse (EV_P_ W w)	2049	feed_reverse (EV_P_ W w)
1714	{	2050	{
1715	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, EMPTY2);	2051	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, array_needsize_noinit);
1716	rfeeds [rfeedcnt++] = w;	2052	rfeeds [rfeedcnt++] = w;
1717	}	2053	}
1718		2054
1719	inline_size void	2055	inline_size void
1720	feed_reverse_done (EV_P_ int revents)	2056	feed_reverse_done (EV_P_ int revents)
…		…
1755	inline_speed void	2091	inline_speed void
1756	fd_event (EV_P_ int fd, int revents)	2092	fd_event (EV_P_ int fd, int revents)
1757	{	2093	{
1758	ANFD *anfd = anfds + fd;	2094	ANFD *anfd = anfds + fd;
1759		2095
1760	if (expect_true (!anfd->reify))	2096	if (ecb_expect_true (!anfd->reify))
1761	fd_event_nocheck (EV_A_ fd, revents);	2097	fd_event_nocheck (EV_A_ fd, revents);
1762	}	2098	}
1763		2099
1764	void	2100	void
1765	ev_feed_fd_event (EV_P_ int fd, int revents) EV_THROW	2101	ev_feed_fd_event (EV_P_ int fd, int revents) EV_NOEXCEPT
1766	{	2102	{
1767	if (fd >= 0 && fd < anfdmax)	2103	if (fd >= 0 && fd < anfdmax)
1768	fd_event_nocheck (EV_A_ fd, revents);	2104	fd_event_nocheck (EV_A_ fd, revents);
1769	}	2105	}
1770		2106
…		…
1807	ev_io *w;	2143	ev_io *w;
1808		2144
1809	unsigned char o_events = anfd->events;	2145	unsigned char o_events = anfd->events;
1810	unsigned char o_reify = anfd->reify;	2146	unsigned char o_reify = anfd->reify;
1811		2147
1812	anfd->reify = 0;	2148	anfd->reify = 0;
1813		2149
1814	/*if (expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */	2150	/*if (ecb_expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */
1815	{	2151	{
1816	anfd->events = 0;	2152	anfd->events = 0;
1817		2153
1818	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)	2154	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)
1819	anfd->events |= (unsigned char)w->events;	2155	anfd->events |= (unsigned char)w->events;
…		…
1828		2164
1829	fdchangecnt = 0;	2165	fdchangecnt = 0;
1830	}	2166	}
1831		2167
1832	/* something about the given fd changed */	2168	/* something about the given fd changed */
1833	inline_size void	2169	inline_size
		2170	void
1834	fd_change (EV_P_ int fd, int flags)	2171	fd_change (EV_P_ int fd, int flags)
1835	{	2172	{
1836	unsigned char reify = anfds [fd].reify;	2173	unsigned char reify = anfds [fd].reify;
1837	anfds [fd].reify |= flags;	2174	anfds [fd].reify |= flags;
1838		2175
1839	if (expect_true (!reify))	2176	if (ecb_expect_true (!reify))
1840	{	2177	{
1841	++fdchangecnt;	2178	++fdchangecnt;
1842	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, EMPTY2);	2179	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, array_needsize_noinit);
1843	fdchanges [fdchangecnt - 1] = fd;	2180	fdchanges [fdchangecnt - 1] = fd;
1844	}	2181	}
1845	}	2182	}
1846		2183
1847	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */	2184	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */
1848	inline_speed void ecb_cold	2185	inline_speed ecb_cold void
1849	fd_kill (EV_P_ int fd)	2186	fd_kill (EV_P_ int fd)
1850	{	2187	{
1851	ev_io *w;	2188	ev_io *w;
1852		2189
1853	while ((w = (ev_io *)anfds [fd].head))	2190	while ((w = (ev_io *)anfds [fd].head))
…		…
1856	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);	2193	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);
1857	}	2194	}
1858	}	2195	}
1859		2196
1860	/* check whether the given fd is actually valid, for error recovery */	2197	/* check whether the given fd is actually valid, for error recovery */
1861	inline_size int ecb_cold	2198	inline_size ecb_cold int
1862	fd_valid (int fd)	2199	fd_valid (int fd)
1863	{	2200	{
1864	#ifdef _WIN32	2201	#ifdef _WIN32
1865	return EV_FD_TO_WIN32_HANDLE (fd) != -1;	2202	return EV_FD_TO_WIN32_HANDLE (fd) != -1;
1866	#else	2203	#else
1867	return fcntl (fd, F_GETFD) != -1;	2204	return fcntl (fd, F_GETFD) != -1;
1868	#endif	2205	#endif
1869	}	2206	}
1870		2207
1871	/* called on EBADF to verify fds */	2208	/* called on EBADF to verify fds */
1872	static void noinline ecb_cold	2209	ecb_noinline ecb_cold
		2210	static void
1873	fd_ebadf (EV_P)	2211	fd_ebadf (EV_P)
1874	{	2212	{
1875	int fd;	2213	int fd;
1876		2214
1877	for (fd = 0; fd < anfdmax; ++fd)	2215	for (fd = 0; fd < anfdmax; ++fd)
…		…
1879	if (!fd_valid (fd) && errno == EBADF)	2217	if (!fd_valid (fd) && errno == EBADF)
1880	fd_kill (EV_A_ fd);	2218	fd_kill (EV_A_ fd);
1881	}	2219	}
1882		2220
1883	/* called on ENOMEM in select/poll to kill some fds and retry */	2221	/* called on ENOMEM in select/poll to kill some fds and retry */
1884	static void noinline ecb_cold	2222	ecb_noinline ecb_cold
		2223	static void
1885	fd_enomem (EV_P)	2224	fd_enomem (EV_P)
1886	{	2225	{
1887	int fd;	2226	int fd;
1888		2227
1889	for (fd = anfdmax; fd--; )	2228	for (fd = anfdmax; fd--; )
…		…
1893	break;	2232	break;
1894	}	2233	}
1895	}	2234	}
1896		2235
1897	/* usually called after fork if backend needs to re-arm all fds from scratch */	2236	/* usually called after fork if backend needs to re-arm all fds from scratch */
1898	static void noinline	2237	ecb_noinline
		2238	static void
1899	fd_rearm_all (EV_P)	2239	fd_rearm_all (EV_P)
1900	{	2240	{
1901	int fd;	2241	int fd;
1902		2242
1903	for (fd = 0; fd < anfdmax; ++fd)	2243	for (fd = 0; fd < anfdmax; ++fd)
…		…
1956	ev_tstamp minat;	2296	ev_tstamp minat;
1957	ANHE *minpos;	2297	ANHE *minpos;
1958	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;	2298	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;
1959		2299
1960	/* find minimum child */	2300	/* find minimum child */
1961	if (expect_true (pos + DHEAP - 1 < E))	2301	if (ecb_expect_true (pos + DHEAP - 1 < E))
1962	{	2302	{
1963	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));	2303	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));
1964	if ( ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));	2304	if ( ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));
1965	if ( ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));	2305	if ( ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));
1966	if ( ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));	2306	if ( ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));
…		…
2084		2424
2085	/*****************************************************************************/	2425	/*****************************************************************************/
2086		2426
2087	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	2427	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2088		2428
2089	static void noinline ecb_cold	2429	ecb_noinline ecb_cold
		2430	static void
2090	evpipe_init (EV_P)	2431	evpipe_init (EV_P)
2091	{	2432	{
2092	if (!ev_is_active (&pipe_w))	2433	if (!ev_is_active (&pipe_w))
2093	{	2434	{
2094	int fds [2];	2435	int fds [2];
…		…
2134	inline_speed void	2475	inline_speed void
2135	evpipe_write (EV_P_ EV_ATOMIC_T *flag)	2476	evpipe_write (EV_P_ EV_ATOMIC_T *flag)
2136	{	2477	{
2137	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */	2478	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */
2138		2479
2139	if (expect_true (*flag))	2480	if (ecb_expect_true (*flag))
2140	return;	2481	return;
2141		2482
2142	*flag = 1;	2483	*flag = 1;
2143	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */	2484	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */
2144		2485
…		…
2165	#endif	2506	#endif
2166	{	2507	{
2167	#ifdef _WIN32	2508	#ifdef _WIN32
2168	WSABUF buf;	2509	WSABUF buf;
2169	DWORD sent;	2510	DWORD sent;
2170	buf.buf = &buf;	2511	buf.buf = (char *)&buf;
2171	buf.len = 1;	2512	buf.len = 1;
2172	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);	2513	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);
2173	#else	2514	#else
2174	write (evpipe [1], &(evpipe [1]), 1);	2515	write (evpipe [1], &(evpipe [1]), 1);
2175	#endif	2516	#endif
…		…
2221	sig_pending = 0;	2562	sig_pending = 0;
2222		2563
2223	ECB_MEMORY_FENCE;	2564	ECB_MEMORY_FENCE;
2224		2565
2225	for (i = EV_NSIG - 1; i--; )	2566	for (i = EV_NSIG - 1; i--; )
2226	if (expect_false (signals [i].pending))	2567	if (ecb_expect_false (signals [i].pending))
2227	ev_feed_signal_event (EV_A_ i + 1);	2568	ev_feed_signal_event (EV_A_ i + 1);
2228	}	2569	}
2229	#endif	2570	#endif
2230		2571
2231	#if EV_ASYNC_ENABLE	2572	#if EV_ASYNC_ENABLE
…		…
2247	}	2588	}
2248		2589
2249	/*****************************************************************************/	2590	/*****************************************************************************/
2250		2591
2251	void	2592	void
2252	ev_feed_signal (int signum) EV_THROW	2593	ev_feed_signal (int signum) EV_NOEXCEPT
2253	{	2594	{
2254	#if EV_MULTIPLICITY	2595	#if EV_MULTIPLICITY
2255	EV_P;	2596	EV_P;
2256	ECB_MEMORY_FENCE_ACQUIRE;	2597	ECB_MEMORY_FENCE_ACQUIRE;
2257	EV_A = signals [signum - 1].loop;	2598	EV_A = signals [signum - 1].loop;
…		…
2272	#endif	2613	#endif
2273		2614
2274	ev_feed_signal (signum);	2615	ev_feed_signal (signum);
2275	}	2616	}
2276		2617
2277	void noinline	2618	ecb_noinline
		2619	void
2278	ev_feed_signal_event (EV_P_ int signum) EV_THROW	2620	ev_feed_signal_event (EV_P_ int signum) EV_NOEXCEPT
2279	{	2621	{
2280	WL w;	2622	WL w;
2281		2623
2282	if (expect_false (signum <= 0 || signum >= EV_NSIG))	2624	if (ecb_expect_false (signum <= 0 || signum >= EV_NSIG))
2283	return;	2625	return;
2284		2626
2285	--signum;	2627	--signum;
2286		2628
2287	#if EV_MULTIPLICITY	2629	#if EV_MULTIPLICITY
2288	/* it is permissible to try to feed a signal to the wrong loop */	2630	/* it is permissible to try to feed a signal to the wrong loop */
2289	/* or, likely more useful, feeding a signal nobody is waiting for */	2631	/* or, likely more useful, feeding a signal nobody is waiting for */
2290		2632
2291	if (expect_false (signals [signum].loop != EV_A))	2633	if (ecb_expect_false (signals [signum].loop != EV_A))
2292	return;	2634	return;
2293	#endif	2635	#endif
2294		2636
2295	signals [signum].pending = 0;	2637	signals [signum].pending = 0;
2296	ECB_MEMORY_FENCE_RELEASE;	2638	ECB_MEMORY_FENCE_RELEASE;
…		…
2392	# include "ev_kqueue.c"	2734	# include "ev_kqueue.c"
2393	#endif	2735	#endif
2394	#if EV_USE_EPOLL	2736	#if EV_USE_EPOLL
2395	# include "ev_epoll.c"	2737	# include "ev_epoll.c"
2396	#endif	2738	#endif
		2739	#if EV_USE_LINUXAIO
		2740	# include "ev_linuxaio.c"
		2741	#endif
2397	#if EV_USE_POLL	2742	#if EV_USE_POLL
2398	# include "ev_poll.c"	2743	# include "ev_poll.c"
2399	#endif	2744	#endif
2400	#if EV_USE_SELECT	2745	#if EV_USE_SELECT
2401	# include "ev_select.c"	2746	# include "ev_select.c"
2402	#endif	2747	#endif
2403		2748
2404	int ecb_cold	2749	ecb_cold int
2405	ev_version_major (void) EV_THROW	2750	ev_version_major (void) EV_NOEXCEPT
2406	{	2751	{
2407	return EV_VERSION_MAJOR;	2752	return EV_VERSION_MAJOR;
2408	}	2753	}
2409		2754
2410	int ecb_cold	2755	ecb_cold int
2411	ev_version_minor (void) EV_THROW	2756	ev_version_minor (void) EV_NOEXCEPT
2412	{	2757	{
2413	return EV_VERSION_MINOR;	2758	return EV_VERSION_MINOR;
2414	}	2759	}
2415		2760
2416	/* return true if we are running with elevated privileges and should ignore env variables */	2761	/* return true if we are running with elevated privileges and should ignore env variables */
2417	int inline_size ecb_cold	2762	inline_size ecb_cold int
2418	enable_secure (void)	2763	enable_secure (void)
2419	{	2764	{
2420	#ifdef _WIN32	2765	#ifdef _WIN32
2421	return 0;	2766	return 0;
2422	#else	2767	#else
2423	return getuid () != geteuid ()	2768	return getuid () != geteuid ()
2424	|| getgid () != getegid ();	2769	|| getgid () != getegid ();
2425	#endif	2770	#endif
2426	}	2771	}
2427		2772
2428	unsigned int ecb_cold	2773	ecb_cold
		2774	unsigned int
2429	ev_supported_backends (void) EV_THROW	2775	ev_supported_backends (void) EV_NOEXCEPT
2430	{	2776	{
2431	unsigned int flags = 0;	2777	unsigned int flags = 0;
2432		2778
2433	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;	2779	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;
2434	if (EV_USE_KQUEUE) flags |= EVBACKEND_KQUEUE;	2780	if (EV_USE_KQUEUE ) flags |= EVBACKEND_KQUEUE;
2435	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;	2781	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;
		2782	if (EV_USE_LINUXAIO) flags |= EVBACKEND_LINUXAIO;
2436	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;	2783	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;
2437	if (EV_USE_SELECT) flags |= EVBACKEND_SELECT;	2784	if (EV_USE_SELECT ) flags |= EVBACKEND_SELECT;
2438		2785
2439	return flags;	2786	return flags;
2440	}	2787	}
2441		2788
2442	unsigned int ecb_cold	2789	ecb_cold
		2790	unsigned int
2443	ev_recommended_backends (void) EV_THROW	2791	ev_recommended_backends (void) EV_NOEXCEPT
2444	{	2792	{
2445	unsigned int flags = ev_supported_backends ();	2793	unsigned int flags = ev_supported_backends ();
2446		2794
2447	#ifndef __NetBSD__	2795	#ifndef __NetBSD__
2448	/* kqueue is borked on everything but netbsd apparently */	2796	/* kqueue is borked on everything but netbsd apparently */
…		…
2456	#endif	2804	#endif
2457	#ifdef __FreeBSD__	2805	#ifdef __FreeBSD__
2458	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */	2806	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */
2459	#endif	2807	#endif
2460		2808
		2809	/* TODO: linuxaio is very experimental */
		2810	#if !EV_RECOMMEND_LINUXAIO
		2811	flags &= ~EVBACKEND_LINUXAIO;
		2812	#endif
		2813
2461	return flags;	2814	return flags;
2462	}	2815	}
2463		2816
2464	unsigned int ecb_cold	2817	ecb_cold
		2818	unsigned int
2465	ev_embeddable_backends (void) EV_THROW	2819	ev_embeddable_backends (void) EV_NOEXCEPT
2466	{	2820	{
2467	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;	2821	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;
2468		2822
2469	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */	2823	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */
2470	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */	2824	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */
…		…
2472		2826
2473	return flags;	2827	return flags;
2474	}	2828	}
2475		2829
2476	unsigned int	2830	unsigned int
2477	ev_backend (EV_P) EV_THROW	2831	ev_backend (EV_P) EV_NOEXCEPT
2478	{	2832	{
2479	return backend;	2833	return backend;
2480	}	2834	}
2481		2835
2482	#if EV_FEATURE_API	2836	#if EV_FEATURE_API
2483	unsigned int	2837	unsigned int
2484	ev_iteration (EV_P) EV_THROW	2838	ev_iteration (EV_P) EV_NOEXCEPT
2485	{	2839	{
2486	return loop_count;	2840	return loop_count;
2487	}	2841	}
2488		2842
2489	unsigned int	2843	unsigned int
2490	ev_depth (EV_P) EV_THROW	2844	ev_depth (EV_P) EV_NOEXCEPT
2491	{	2845	{
2492	return loop_depth;	2846	return loop_depth;
2493	}	2847	}
2494		2848
2495	void	2849	void
2496	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2850	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2497	{	2851	{
2498	io_blocktime = interval;	2852	io_blocktime = interval;
2499	}	2853	}
2500		2854
2501	void	2855	void
2502	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2856	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2503	{	2857	{
2504	timeout_blocktime = interval;	2858	timeout_blocktime = interval;
2505	}	2859	}
2506		2860
2507	void	2861	void
2508	ev_set_userdata (EV_P_ void *data) EV_THROW	2862	ev_set_userdata (EV_P_ void *data) EV_NOEXCEPT
2509	{	2863	{
2510	userdata = data;	2864	userdata = data;
2511	}	2865	}
2512		2866
2513	void *	2867	void *
2514	ev_userdata (EV_P) EV_THROW	2868	ev_userdata (EV_P) EV_NOEXCEPT
2515	{	2869	{
2516	return userdata;	2870	return userdata;
2517	}	2871	}
2518		2872
2519	void	2873	void
2520	ev_set_invoke_pending_cb (EV_P_ void (*invoke_pending_cb)(EV_P)) EV_THROW	2874	ev_set_invoke_pending_cb (EV_P_ ev_loop_callback invoke_pending_cb) EV_NOEXCEPT
2521	{	2875	{
2522	invoke_cb = invoke_pending_cb;	2876	invoke_cb = invoke_pending_cb;
2523	}	2877	}
2524		2878
2525	void	2879	void
2526	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_THROW, void (*acquire)(EV_P) EV_THROW) EV_THROW	2880	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_NOEXCEPT, void (*acquire)(EV_P) EV_NOEXCEPT) EV_NOEXCEPT
2527	{	2881	{
2528	release_cb = release;	2882	release_cb = release;
2529	acquire_cb = acquire;	2883	acquire_cb = acquire;
2530	}	2884	}
2531	#endif	2885	#endif
2532		2886
2533	/* initialise a loop structure, must be zero-initialised */	2887	/* initialise a loop structure, must be zero-initialised */
2534	static void noinline ecb_cold	2888	ecb_noinline ecb_cold
		2889	static void
2535	loop_init (EV_P_ unsigned int flags) EV_THROW	2890	loop_init (EV_P_ unsigned int flags) EV_NOEXCEPT
2536	{	2891	{
2537	if (!backend)	2892	if (!backend)
2538	{	2893	{
2539	origflags = flags;	2894	origflags = flags;
2540		2895
…		…
2598		2953
2599	if (!(flags & EVBACKEND_MASK))	2954	if (!(flags & EVBACKEND_MASK))
2600	flags |= ev_recommended_backends ();	2955	flags |= ev_recommended_backends ();
2601		2956
2602	#if EV_USE_IOCP	2957	#if EV_USE_IOCP
2603	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);	2958	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);
2604	#endif	2959	#endif
2605	#if EV_USE_PORT	2960	#if EV_USE_PORT
2606	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);	2961	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);
2607	#endif	2962	#endif
2608	#if EV_USE_KQUEUE	2963	#if EV_USE_KQUEUE
2609	if (!backend && (flags & EVBACKEND_KQUEUE)) backend = kqueue_init (EV_A_ flags);	2964	if (!backend && (flags & EVBACKEND_KQUEUE )) backend = kqueue_init (EV_A_ flags);
		2965	#endif
		2966	#if EV_USE_LINUXAIO
		2967	if (!backend && (flags & EVBACKEND_LINUXAIO)) backend = linuxaio_init (EV_A_ flags);
2610	#endif	2968	#endif
2611	#if EV_USE_EPOLL	2969	#if EV_USE_EPOLL
2612	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);	2970	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);
2613	#endif	2971	#endif
2614	#if EV_USE_POLL	2972	#if EV_USE_POLL
2615	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);	2973	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);
2616	#endif	2974	#endif
2617	#if EV_USE_SELECT	2975	#if EV_USE_SELECT
2618	if (!backend && (flags & EVBACKEND_SELECT)) backend = select_init (EV_A_ flags);	2976	if (!backend && (flags & EVBACKEND_SELECT )) backend = select_init (EV_A_ flags);
2619	#endif	2977	#endif
2620		2978
2621	ev_prepare_init (&pending_w, pendingcb);	2979	ev_prepare_init (&pending_w, pendingcb);
2622		2980
2623	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	2981	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
…		…
2626	#endif	2984	#endif
2627	}	2985	}
2628	}	2986	}
2629		2987
2630	/* free up a loop structure */	2988	/* free up a loop structure */
2631	void ecb_cold	2989	ecb_cold
		2990	void
2632	ev_loop_destroy (EV_P)	2991	ev_loop_destroy (EV_P)
2633	{	2992	{
2634	int i;	2993	int i;
2635		2994
2636	#if EV_MULTIPLICITY	2995	#if EV_MULTIPLICITY
…		…
2639	return;	2998	return;
2640	#endif	2999	#endif
2641		3000
2642	#if EV_CLEANUP_ENABLE	3001	#if EV_CLEANUP_ENABLE
2643	/* queue cleanup watchers (and execute them) */	3002	/* queue cleanup watchers (and execute them) */
2644	if (expect_false (cleanupcnt))	3003	if (ecb_expect_false (cleanupcnt))
2645	{	3004	{
2646	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);	3005	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);
2647	EV_INVOKE_PENDING;	3006	EV_INVOKE_PENDING;
2648	}	3007	}
2649	#endif	3008	#endif
…		…
2677		3036
2678	if (backend_fd >= 0)	3037	if (backend_fd >= 0)
2679	close (backend_fd);	3038	close (backend_fd);
2680		3039
2681	#if EV_USE_IOCP	3040	#if EV_USE_IOCP
2682	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);	3041	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);
2683	#endif	3042	#endif
2684	#if EV_USE_PORT	3043	#if EV_USE_PORT
2685	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);	3044	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);
2686	#endif	3045	#endif
2687	#if EV_USE_KQUEUE	3046	#if EV_USE_KQUEUE
2688	if (backend == EVBACKEND_KQUEUE) kqueue_destroy (EV_A);	3047	if (backend == EVBACKEND_KQUEUE ) kqueue_destroy (EV_A);
		3048	#endif
		3049	#if EV_USE_LINUXAIO
		3050	if (backend == EVBACKEND_LINUXAIO) linuxaio_destroy (EV_A);
2689	#endif	3051	#endif
2690	#if EV_USE_EPOLL	3052	#if EV_USE_EPOLL
2691	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);	3053	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);
2692	#endif	3054	#endif
2693	#if EV_USE_POLL	3055	#if EV_USE_POLL
2694	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);	3056	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);
2695	#endif	3057	#endif
2696	#if EV_USE_SELECT	3058	#if EV_USE_SELECT
2697	if (backend == EVBACKEND_SELECT) select_destroy (EV_A);	3059	if (backend == EVBACKEND_SELECT ) select_destroy (EV_A);
2698	#endif	3060	#endif
2699		3061
2700	for (i = NUMPRI; i--; )	3062	for (i = NUMPRI; i--; )
2701	{	3063	{
2702	array_free (pending, [i]);	3064	array_free (pending, [i]);
…		…
2744		3106
2745	inline_size void	3107	inline_size void
2746	loop_fork (EV_P)	3108	loop_fork (EV_P)
2747	{	3109	{
2748	#if EV_USE_PORT	3110	#if EV_USE_PORT
2749	if (backend == EVBACKEND_PORT ) port_fork (EV_A);	3111	if (backend == EVBACKEND_PORT ) port_fork (EV_A);
2750	#endif	3112	#endif
2751	#if EV_USE_KQUEUE	3113	#if EV_USE_KQUEUE
2752	if (backend == EVBACKEND_KQUEUE) kqueue_fork (EV_A);	3114	if (backend == EVBACKEND_KQUEUE ) kqueue_fork (EV_A);
		3115	#endif
		3116	#if EV_USE_LINUXAIO
		3117	if (backend == EVBACKEND_LINUXAIO) linuxaio_fork (EV_A);
2753	#endif	3118	#endif
2754	#if EV_USE_EPOLL	3119	#if EV_USE_EPOLL
2755	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);	3120	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);
2756	#endif	3121	#endif
2757	#if EV_USE_INOTIFY	3122	#if EV_USE_INOTIFY
2758	infy_fork (EV_A);	3123	infy_fork (EV_A);
2759	#endif	3124	#endif
2760		3125
2761	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	3126	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2762	if (ev_is_active (&pipe_w))	3127	if (ev_is_active (&pipe_w) && postfork != 2)
2763	{	3128	{
2764	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */	3129	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */
2765		3130
2766	ev_ref (EV_A);	3131	ev_ref (EV_A);
2767	ev_io_stop (EV_A_ &pipe_w);	3132	ev_io_stop (EV_A_ &pipe_w);
…		…
2778	postfork = 0;	3143	postfork = 0;
2779	}	3144	}
2780		3145
2781	#if EV_MULTIPLICITY	3146	#if EV_MULTIPLICITY
2782		3147
		3148	ecb_cold
2783	struct ev_loop * ecb_cold	3149	struct ev_loop *
2784	ev_loop_new (unsigned int flags) EV_THROW	3150	ev_loop_new (unsigned int flags) EV_NOEXCEPT
2785	{	3151	{
2786	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));	3152	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));
2787		3153
2788	memset (EV_A, 0, sizeof (struct ev_loop));	3154	memset (EV_A, 0, sizeof (struct ev_loop));
2789	loop_init (EV_A_ flags);	3155	loop_init (EV_A_ flags);
…		…
2796	}	3162	}
2797		3163
2798	#endif /* multiplicity */	3164	#endif /* multiplicity */
2799		3165
2800	#if EV_VERIFY	3166	#if EV_VERIFY
2801	static void noinline ecb_cold	3167	ecb_noinline ecb_cold
		3168	static void
2802	verify_watcher (EV_P_ W w)	3169	verify_watcher (EV_P_ W w)
2803	{	3170	{
2804	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));	3171	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));
2805		3172
2806	if (w->pending)	3173	if (w->pending)
2807	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));	3174	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));
2808	}	3175	}
2809		3176
2810	static void noinline ecb_cold	3177	ecb_noinline ecb_cold
		3178	static void
2811	verify_heap (EV_P_ ANHE *heap, int N)	3179	verify_heap (EV_P_ ANHE *heap, int N)
2812	{	3180	{
2813	int i;	3181	int i;
2814		3182
2815	for (i = HEAP0; i < N + HEAP0; ++i)	3183	for (i = HEAP0; i < N + HEAP0; ++i)
…		…
2820		3188
2821	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));	3189	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));
2822	}	3190	}
2823	}	3191	}
2824		3192
2825	static void noinline ecb_cold	3193	ecb_noinline ecb_cold
		3194	static void
2826	array_verify (EV_P_ W *ws, int cnt)	3195	array_verify (EV_P_ W *ws, int cnt)
2827	{	3196	{
2828	while (cnt--)	3197	while (cnt--)
2829	{	3198	{
2830	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));	3199	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));
…		…
2833	}	3202	}
2834	#endif	3203	#endif
2835		3204
2836	#if EV_FEATURE_API	3205	#if EV_FEATURE_API
2837	void ecb_cold	3206	void ecb_cold
2838	ev_verify (EV_P) EV_THROW	3207	ev_verify (EV_P) EV_NOEXCEPT
2839	{	3208	{
2840	#if EV_VERIFY	3209	#if EV_VERIFY
2841	int i;	3210	int i;
2842	WL w, w2;	3211	WL w, w2;
2843		3212
…		…
2919	#endif	3288	#endif
2920	}	3289	}
2921	#endif	3290	#endif
2922		3291
2923	#if EV_MULTIPLICITY	3292	#if EV_MULTIPLICITY
		3293	ecb_cold
2924	struct ev_loop * ecb_cold	3294	struct ev_loop *
2925	#else	3295	#else
2926	int	3296	int
2927	#endif	3297	#endif
2928	ev_default_loop (unsigned int flags) EV_THROW	3298	ev_default_loop (unsigned int flags) EV_NOEXCEPT
2929	{	3299	{
2930	if (!ev_default_loop_ptr)	3300	if (!ev_default_loop_ptr)
2931	{	3301	{
2932	#if EV_MULTIPLICITY	3302	#if EV_MULTIPLICITY
2933	EV_P = ev_default_loop_ptr = &default_loop_struct;	3303	EV_P = ev_default_loop_ptr = &default_loop_struct;
…		…
2952		3322
2953	return ev_default_loop_ptr;	3323	return ev_default_loop_ptr;
2954	}	3324	}
2955		3325
2956	void	3326	void
2957	ev_loop_fork (EV_P) EV_THROW	3327	ev_loop_fork (EV_P) EV_NOEXCEPT
2958	{	3328	{
2959	postfork = 1;	3329	postfork = 1;
2960	}	3330	}
2961		3331
2962	/*****************************************************************************/	3332	/*****************************************************************************/
…		…
2966	{	3336	{
2967	EV_CB_INVOKE ((W)w, revents);	3337	EV_CB_INVOKE ((W)w, revents);
2968	}	3338	}
2969		3339
2970	unsigned int	3340	unsigned int
2971	ev_pending_count (EV_P) EV_THROW	3341	ev_pending_count (EV_P) EV_NOEXCEPT
2972	{	3342	{
2973	int pri;	3343	int pri;
2974	unsigned int count = 0;	3344	unsigned int count = 0;
2975		3345
2976	for (pri = NUMPRI; pri--; )	3346	for (pri = NUMPRI; pri--; )
2977	count += pendingcnt [pri];	3347	count += pendingcnt [pri];
2978		3348
2979	return count;	3349	return count;
2980	}	3350	}
2981		3351
2982	void noinline	3352	ecb_noinline
		3353	void
2983	ev_invoke_pending (EV_P)	3354	ev_invoke_pending (EV_P)
2984	{	3355	{
2985	pendingpri = NUMPRI;	3356	pendingpri = NUMPRI;
2986		3357
2987	while (pendingpri) /* pendingpri possibly gets modified in the inner loop */	3358	do
2988	{	3359	{
2989	--pendingpri;	3360	--pendingpri;
2990		3361
		3362	/* pendingpri possibly gets modified in the inner loop */
2991	while (pendingcnt [pendingpri])	3363	while (pendingcnt [pendingpri])
2992	{	3364	{
2993	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];	3365	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];
2994		3366
2995	p->w->pending = 0;	3367	p->w->pending = 0;
2996	EV_CB_INVOKE (p->w, p->events);	3368	EV_CB_INVOKE (p->w, p->events);
2997	EV_FREQUENT_CHECK;	3369	EV_FREQUENT_CHECK;
2998	}	3370	}
2999	}	3371	}
		3372	while (pendingpri);
3000	}	3373	}
3001		3374
3002	#if EV_IDLE_ENABLE	3375	#if EV_IDLE_ENABLE
3003	/* make idle watchers pending. this handles the "call-idle */	3376	/* make idle watchers pending. this handles the "call-idle */
3004	/* only when higher priorities are idle" logic */	3377	/* only when higher priorities are idle" logic */
3005	inline_size void	3378	inline_size void
3006	idle_reify (EV_P)	3379	idle_reify (EV_P)
3007	{	3380	{
3008	if (expect_false (idleall))	3381	if (ecb_expect_false (idleall))
3009	{	3382	{
3010	int pri;	3383	int pri;
3011		3384
3012	for (pri = NUMPRI; pri--; )	3385	for (pri = NUMPRI; pri--; )
3013	{	3386	{
…		…
3062	}	3435	}
3063	}	3436	}
3064		3437
3065	#if EV_PERIODIC_ENABLE	3438	#if EV_PERIODIC_ENABLE
3066		3439
3067	static void noinline	3440	ecb_noinline
		3441	static void
3068	periodic_recalc (EV_P_ ev_periodic *w)	3442	periodic_recalc (EV_P_ ev_periodic *w)
3069	{	3443	{
3070	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;	3444	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;
3071	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);	3445	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);
3072		3446
…		…
3074	while (at <= ev_rt_now)	3448	while (at <= ev_rt_now)
3075	{	3449	{
3076	ev_tstamp nat = at + w->interval;	3450	ev_tstamp nat = at + w->interval;
3077		3451
3078	/* when resolution fails us, we use ev_rt_now */	3452	/* when resolution fails us, we use ev_rt_now */
3079	if (expect_false (nat == at))	3453	if (ecb_expect_false (nat == at))
3080	{	3454	{
3081	at = ev_rt_now;	3455	at = ev_rt_now;
3082	break;	3456	break;
3083	}	3457	}
3084		3458
…		…
3130	}	3504	}
3131	}	3505	}
3132		3506
3133	/* simply recalculate all periodics */	3507	/* simply recalculate all periodics */
3134	/* TODO: maybe ensure that at least one event happens when jumping forward? */	3508	/* TODO: maybe ensure that at least one event happens when jumping forward? */
3135	static void noinline ecb_cold	3509	ecb_noinline ecb_cold
		3510	static void
3136	periodics_reschedule (EV_P)	3511	periodics_reschedule (EV_P)
3137	{	3512	{
3138	int i;	3513	int i;
3139		3514
3140	/* adjust periodics after time jump */	3515	/* adjust periodics after time jump */
…		…
3153	reheap (periodics, periodiccnt);	3528	reheap (periodics, periodiccnt);
3154	}	3529	}
3155	#endif	3530	#endif
3156		3531
3157	/* adjust all timers by a given offset */	3532	/* adjust all timers by a given offset */
3158	static void noinline ecb_cold	3533	ecb_noinline ecb_cold
		3534	static void
3159	timers_reschedule (EV_P_ ev_tstamp adjust)	3535	timers_reschedule (EV_P_ ev_tstamp adjust)
3160	{	3536	{
3161	int i;	3537	int i;
3162		3538
3163	for (i = 0; i < timercnt; ++i)	3539	for (i = 0; i < timercnt; ++i)
…		…
3172	/* also detect if there was a timejump, and act accordingly */	3548	/* also detect if there was a timejump, and act accordingly */
3173	inline_speed void	3549	inline_speed void
3174	time_update (EV_P_ ev_tstamp max_block)	3550	time_update (EV_P_ ev_tstamp max_block)
3175	{	3551	{
3176	#if EV_USE_MONOTONIC	3552	#if EV_USE_MONOTONIC
3177	if (expect_true (have_monotonic))	3553	if (ecb_expect_true (have_monotonic))
3178	{	3554	{
3179	int i;	3555	int i;
3180	ev_tstamp odiff = rtmn_diff;	3556	ev_tstamp odiff = rtmn_diff;
3181		3557
3182	mn_now = get_clock ();	3558	mn_now = get_clock ();
3183		3559
3184	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */	3560	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */
3185	/* interpolate in the meantime */	3561	/* interpolate in the meantime */
3186	if (expect_true (mn_now - now_floor < MIN_TIMEJUMP * .5))	3562	if (ecb_expect_true (mn_now - now_floor < MIN_TIMEJUMP * .5))
3187	{	3563	{
3188	ev_rt_now = rtmn_diff + mn_now;	3564	ev_rt_now = rtmn_diff + mn_now;
3189	return;	3565	return;
3190	}	3566	}
3191		3567
…		…
3205	ev_tstamp diff;	3581	ev_tstamp diff;
3206	rtmn_diff = ev_rt_now - mn_now;	3582	rtmn_diff = ev_rt_now - mn_now;
3207		3583
3208	diff = odiff - rtmn_diff;	3584	diff = odiff - rtmn_diff;
3209		3585
3210	if (expect_true ((diff < 0. ? -diff : diff) < MIN_TIMEJUMP))	3586	if (ecb_expect_true ((diff < 0. ? -diff : diff) < MIN_TIMEJUMP))
3211	return; /* all is well */	3587	return; /* all is well */
3212		3588
3213	ev_rt_now = ev_time ();	3589	ev_rt_now = ev_time ();
3214	mn_now = get_clock ();	3590	mn_now = get_clock ();
3215	now_floor = mn_now;	3591	now_floor = mn_now;
…		…
3224	else	3600	else
3225	#endif	3601	#endif
3226	{	3602	{
3227	ev_rt_now = ev_time ();	3603	ev_rt_now = ev_time ();
3228		3604
3229	if (expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + MIN_TIMEJUMP))	3605	if (ecb_expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + MIN_TIMEJUMP))
3230	{	3606	{
3231	/* adjust timers. this is easy, as the offset is the same for all of them */	3607	/* adjust timers. this is easy, as the offset is the same for all of them */
3232	timers_reschedule (EV_A_ ev_rt_now - mn_now);	3608	timers_reschedule (EV_A_ ev_rt_now - mn_now);
3233	#if EV_PERIODIC_ENABLE	3609	#if EV_PERIODIC_ENABLE
3234	periodics_reschedule (EV_A);	3610	periodics_reschedule (EV_A);
…		…
3257	#if EV_VERIFY >= 2	3633	#if EV_VERIFY >= 2
3258	ev_verify (EV_A);	3634	ev_verify (EV_A);
3259	#endif	3635	#endif
3260		3636
3261	#ifndef _WIN32	3637	#ifndef _WIN32
3262	if (expect_false (curpid)) /* penalise the forking check even more */	3638	if (ecb_expect_false (curpid)) /* penalise the forking check even more */
3263	if (expect_false (getpid () != curpid))	3639	if (ecb_expect_false (getpid () != curpid))
3264	{	3640	{
3265	curpid = getpid ();	3641	curpid = getpid ();
3266	postfork = 1;	3642	postfork = 1;
3267	}	3643	}
3268	#endif	3644	#endif
3269		3645
3270	#if EV_FORK_ENABLE	3646	#if EV_FORK_ENABLE
3271	/* we might have forked, so queue fork handlers */	3647	/* we might have forked, so queue fork handlers */
3272	if (expect_false (postfork))	3648	if (ecb_expect_false (postfork))
3273	if (forkcnt)	3649	if (forkcnt)
3274	{	3650	{
3275	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);	3651	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);
3276	EV_INVOKE_PENDING;	3652	EV_INVOKE_PENDING;
3277	}	3653	}
3278	#endif	3654	#endif
3279		3655
3280	#if EV_PREPARE_ENABLE	3656	#if EV_PREPARE_ENABLE
3281	/* queue prepare watchers (and execute them) */	3657	/* queue prepare watchers (and execute them) */
3282	if (expect_false (preparecnt))	3658	if (ecb_expect_false (preparecnt))
3283	{	3659	{
3284	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);	3660	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);
3285	EV_INVOKE_PENDING;	3661	EV_INVOKE_PENDING;
3286	}	3662	}
3287	#endif	3663	#endif
3288		3664
3289	if (expect_false (loop_done))	3665	if (ecb_expect_false (loop_done))
3290	break;	3666	break;
3291		3667
3292	/* we might have forked, so reify kernel state if necessary */	3668	/* we might have forked, so reify kernel state if necessary */
3293	if (expect_false (postfork))	3669	if (ecb_expect_false (postfork))
3294	loop_fork (EV_A);	3670	loop_fork (EV_A);
3295		3671
3296	/* update fd-related kernel structures */	3672	/* update fd-related kernel structures */
3297	fd_reify (EV_A);	3673	fd_reify (EV_A);
3298		3674
…		…
3310	/* from now on, we want a pipe-wake-up */	3686	/* from now on, we want a pipe-wake-up */
3311	pipe_write_wanted = 1;	3687	pipe_write_wanted = 1;
3312		3688
3313	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */	3689	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */
3314		3690
3315	if (expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))	3691	if (ecb_expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))
3316	{	3692	{
3317	waittime = MAX_BLOCKTIME;	3693	waittime = MAX_BLOCKTIME;
3318		3694
3319	if (timercnt)	3695	if (timercnt)
3320	{	3696	{
…		…
3329	if (waittime > to) waittime = to;	3705	if (waittime > to) waittime = to;
3330	}	3706	}
3331	#endif	3707	#endif
3332		3708
3333	/* don't let timeouts decrease the waittime below timeout_blocktime */	3709	/* don't let timeouts decrease the waittime below timeout_blocktime */
3334	if (expect_false (waittime < timeout_blocktime))	3710	if (ecb_expect_false (waittime < timeout_blocktime))
3335	waittime = timeout_blocktime;	3711	waittime = timeout_blocktime;
3336		3712
3337	/* at this point, we NEED to wait, so we have to ensure */	3713	/* at this point, we NEED to wait, so we have to ensure */
3338	/* to pass a minimum nonzero value to the backend */	3714	/* to pass a minimum nonzero value to the backend */
3339	if (expect_false (waittime < backend_mintime))	3715	if (ecb_expect_false (waittime < backend_mintime))
3340	waittime = backend_mintime;	3716	waittime = backend_mintime;
3341		3717
3342	/* extra check because io_blocktime is commonly 0 */	3718	/* extra check because io_blocktime is commonly 0 */
3343	if (expect_false (io_blocktime))	3719	if (ecb_expect_false (io_blocktime))
3344	{	3720	{
3345	sleeptime = io_blocktime - (mn_now - prev_mn_now);	3721	sleeptime = io_blocktime - (mn_now - prev_mn_now);
3346		3722
3347	if (sleeptime > waittime - backend_mintime)	3723	if (sleeptime > waittime - backend_mintime)
3348	sleeptime = waittime - backend_mintime;	3724	sleeptime = waittime - backend_mintime;
3349		3725
3350	if (expect_true (sleeptime > 0.))	3726	if (ecb_expect_true (sleeptime > 0.))
3351	{	3727	{
3352	ev_sleep (sleeptime);	3728	ev_sleep (sleeptime);
3353	waittime -= sleeptime;	3729	waittime -= sleeptime;
3354	}	3730	}
3355	}	3731	}
…		…
3369	{	3745	{
3370	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));	3746	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));
3371	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);	3747	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);
3372	}	3748	}
3373		3749
3374
3375	/* update ev_rt_now, do magic */	3750	/* update ev_rt_now, do magic */
3376	time_update (EV_A_ waittime + sleeptime);	3751	time_update (EV_A_ waittime + sleeptime);
3377	}	3752	}
3378		3753
3379	/* queue pending timers and reschedule them */	3754	/* queue pending timers and reschedule them */
…		…
3387	idle_reify (EV_A);	3762	idle_reify (EV_A);
3388	#endif	3763	#endif
3389		3764
3390	#if EV_CHECK_ENABLE	3765	#if EV_CHECK_ENABLE
3391	/* queue check watchers, to be executed first */	3766	/* queue check watchers, to be executed first */
3392	if (expect_false (checkcnt))	3767	if (ecb_expect_false (checkcnt))
3393	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);	3768	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);
3394	#endif	3769	#endif
3395		3770
3396	EV_INVOKE_PENDING;	3771	EV_INVOKE_PENDING;
3397	}	3772	}
3398	while (expect_true (	3773	while (ecb_expect_true (
3399	activecnt	3774	activecnt
3400	&& !loop_done	3775	&& !loop_done
3401	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))	3776	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))
3402	));	3777	));
3403		3778
…		…
3410		3785
3411	return activecnt;	3786	return activecnt;
3412	}	3787	}
3413		3788
3414	void	3789	void
3415	ev_break (EV_P_ int how) EV_THROW	3790	ev_break (EV_P_ int how) EV_NOEXCEPT
3416	{	3791	{
3417	loop_done = how;	3792	loop_done = how;
3418	}	3793	}
3419		3794
3420	void	3795	void
3421	ev_ref (EV_P) EV_THROW	3796	ev_ref (EV_P) EV_NOEXCEPT
3422	{	3797	{
3423	++activecnt;	3798	++activecnt;
3424	}	3799	}
3425		3800
3426	void	3801	void
3427	ev_unref (EV_P) EV_THROW	3802	ev_unref (EV_P) EV_NOEXCEPT
3428	{	3803	{
3429	--activecnt;	3804	--activecnt;
3430	}	3805	}
3431		3806
3432	void	3807	void
3433	ev_now_update (EV_P) EV_THROW	3808	ev_now_update (EV_P) EV_NOEXCEPT
3434	{	3809	{
3435	time_update (EV_A_ 1e100);	3810	time_update (EV_A_ 1e100);
3436	}	3811	}
3437		3812
3438	void	3813	void
3439	ev_suspend (EV_P) EV_THROW	3814	ev_suspend (EV_P) EV_NOEXCEPT
3440	{	3815	{
3441	ev_now_update (EV_A);	3816	ev_now_update (EV_A);
3442	}	3817	}
3443		3818
3444	void	3819	void
3445	ev_resume (EV_P) EV_THROW	3820	ev_resume (EV_P) EV_NOEXCEPT
3446	{	3821	{
3447	ev_tstamp mn_prev = mn_now;	3822	ev_tstamp mn_prev = mn_now;
3448		3823
3449	ev_now_update (EV_A);	3824	ev_now_update (EV_A);
3450	timers_reschedule (EV_A_ mn_now - mn_prev);	3825	timers_reschedule (EV_A_ mn_now - mn_prev);
…		…
3467	inline_size void	3842	inline_size void
3468	wlist_del (WL *head, WL elem)	3843	wlist_del (WL *head, WL elem)
3469	{	3844	{
3470	while (*head)	3845	while (*head)
3471	{	3846	{
3472	if (expect_true (*head == elem))	3847	if (ecb_expect_true (*head == elem))
3473	{	3848	{
3474	*head = elem->next;	3849	*head = elem->next;
3475	break;	3850	break;
3476	}	3851	}
3477		3852
…		…
3489	w->pending = 0;	3864	w->pending = 0;
3490	}	3865	}
3491	}	3866	}
3492		3867
3493	int	3868	int
3494	ev_clear_pending (EV_P_ void *w) EV_THROW	3869	ev_clear_pending (EV_P_ void *w) EV_NOEXCEPT
3495	{	3870	{
3496	W w_ = (W)w;	3871	W w_ = (W)w;
3497	int pending = w_->pending;	3872	int pending = w_->pending;
3498		3873
3499	if (expect_true (pending))	3874	if (ecb_expect_true (pending))
3500	{	3875	{
3501	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;	3876	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;
3502	p->w = (W)&pending_w;	3877	p->w = (W)&pending_w;
3503	w_->pending = 0;	3878	w_->pending = 0;
3504	return p->events;	3879	return p->events;
…		…
3531	w->active = 0;	3906	w->active = 0;
3532	}	3907	}
3533		3908
3534	/*****************************************************************************/	3909	/*****************************************************************************/
3535		3910
3536	void noinline	3911	ecb_noinline
		3912	void
3537	ev_io_start (EV_P_ ev_io *w) EV_THROW	3913	ev_io_start (EV_P_ ev_io *w) EV_NOEXCEPT
3538	{	3914	{
3539	int fd = w->fd;	3915	int fd = w->fd;
3540		3916
3541	if (expect_false (ev_is_active (w)))	3917	if (ecb_expect_false (ev_is_active (w)))
3542	return;	3918	return;
3543		3919
3544	assert (("libev: ev_io_start called with negative fd", fd >= 0));	3920	assert (("libev: ev_io_start called with negative fd", fd >= 0));
3545	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));	3921	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));
3546		3922
		3923	#if EV_VERIFY >= 2
		3924	assert (("libev: ev_io_start called on watcher with invalid fd", fd_valid (fd)));
		3925	#endif
3547	EV_FREQUENT_CHECK;	3926	EV_FREQUENT_CHECK;
3548		3927
3549	ev_start (EV_A_ (W)w, 1);	3928	ev_start (EV_A_ (W)w, 1);
3550	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_init_zero);	3929	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_needsize_zerofill);
3551	wlist_add (&anfds[fd].head, (WL)w);	3930	wlist_add (&anfds[fd].head, (WL)w);
3552		3931
3553	/* common bug, apparently */	3932	/* common bug, apparently */
3554	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));	3933	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));
3555		3934
…		…
3557	w->events &= ~EV__IOFDSET;	3936	w->events &= ~EV__IOFDSET;
3558		3937
3559	EV_FREQUENT_CHECK;	3938	EV_FREQUENT_CHECK;
3560	}	3939	}
3561		3940
3562	void noinline	3941	ecb_noinline
		3942	void
3563	ev_io_stop (EV_P_ ev_io *w) EV_THROW	3943	ev_io_stop (EV_P_ ev_io *w) EV_NOEXCEPT
3564	{	3944	{
3565	clear_pending (EV_A_ (W)w);	3945	clear_pending (EV_A_ (W)w);
3566	if (expect_false (!ev_is_active (w)))	3946	if (ecb_expect_false (!ev_is_active (w)))
3567	return;	3947	return;
3568		3948
3569	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));	3949	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));
3570		3950
		3951	#if EV_VERIFY >= 2
		3952	assert (("libev: ev_io_stop called on watcher with invalid fd", fd_valid (w->fd)));
		3953	#endif
3571	EV_FREQUENT_CHECK;	3954	EV_FREQUENT_CHECK;
3572		3955
3573	wlist_del (&anfds[w->fd].head, (WL)w);	3956	wlist_del (&anfds[w->fd].head, (WL)w);
3574	ev_stop (EV_A_ (W)w);	3957	ev_stop (EV_A_ (W)w);
3575		3958
3576	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);	3959	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);
3577		3960
3578	EV_FREQUENT_CHECK;	3961	EV_FREQUENT_CHECK;
3579	}	3962	}
3580		3963
3581	void noinline	3964	ecb_noinline
		3965	void
3582	ev_timer_start (EV_P_ ev_timer *w) EV_THROW	3966	ev_timer_start (EV_P_ ev_timer *w) EV_NOEXCEPT
3583	{	3967	{
3584	if (expect_false (ev_is_active (w)))	3968	if (ecb_expect_false (ev_is_active (w)))
3585	return;	3969	return;
3586		3970
3587	ev_at (w) += mn_now;	3971	ev_at (w) += mn_now;
3588		3972
3589	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));	3973	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));
3590		3974
3591	EV_FREQUENT_CHECK;	3975	EV_FREQUENT_CHECK;
3592		3976
3593	++timercnt;	3977	++timercnt;
3594	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);	3978	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);
3595	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, EMPTY2);	3979	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, array_needsize_noinit);
3596	ANHE_w (timers [ev_active (w)]) = (WT)w;	3980	ANHE_w (timers [ev_active (w)]) = (WT)w;
3597	ANHE_at_cache (timers [ev_active (w)]);	3981	ANHE_at_cache (timers [ev_active (w)]);
3598	upheap (timers, ev_active (w));	3982	upheap (timers, ev_active (w));
3599		3983
3600	EV_FREQUENT_CHECK;	3984	EV_FREQUENT_CHECK;
3601		3985
3602	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/	3986	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/
3603	}	3987	}
3604		3988
3605	void noinline	3989	ecb_noinline
		3990	void
3606	ev_timer_stop (EV_P_ ev_timer *w) EV_THROW	3991	ev_timer_stop (EV_P_ ev_timer *w) EV_NOEXCEPT
3607	{	3992	{
3608	clear_pending (EV_A_ (W)w);	3993	clear_pending (EV_A_ (W)w);
3609	if (expect_false (!ev_is_active (w)))	3994	if (ecb_expect_false (!ev_is_active (w)))
3610	return;	3995	return;
3611		3996
3612	EV_FREQUENT_CHECK;	3997	EV_FREQUENT_CHECK;
3613		3998
3614	{	3999	{
…		…
3616		4001
3617	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));	4002	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));
3618		4003
3619	--timercnt;	4004	--timercnt;
3620		4005
3621	if (expect_true (active < timercnt + HEAP0))	4006	if (ecb_expect_true (active < timercnt + HEAP0))
3622	{	4007	{
3623	timers [active] = timers [timercnt + HEAP0];	4008	timers [active] = timers [timercnt + HEAP0];
3624	adjustheap (timers, timercnt, active);	4009	adjustheap (timers, timercnt, active);
3625	}	4010	}
3626	}	4011	}
…		…
3630	ev_stop (EV_A_ (W)w);	4015	ev_stop (EV_A_ (W)w);
3631		4016
3632	EV_FREQUENT_CHECK;	4017	EV_FREQUENT_CHECK;
3633	}	4018	}
3634		4019
3635	void noinline	4020	ecb_noinline
		4021	void
3636	ev_timer_again (EV_P_ ev_timer *w) EV_THROW	4022	ev_timer_again (EV_P_ ev_timer *w) EV_NOEXCEPT
3637	{	4023	{
3638	EV_FREQUENT_CHECK;	4024	EV_FREQUENT_CHECK;
3639		4025
3640	clear_pending (EV_A_ (W)w);	4026	clear_pending (EV_A_ (W)w);
3641		4027
…		…
3658		4044
3659	EV_FREQUENT_CHECK;	4045	EV_FREQUENT_CHECK;
3660	}	4046	}
3661		4047
3662	ev_tstamp	4048	ev_tstamp
3663	ev_timer_remaining (EV_P_ ev_timer *w) EV_THROW	4049	ev_timer_remaining (EV_P_ ev_timer *w) EV_NOEXCEPT
3664	{	4050	{
3665	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);	4051	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);
3666	}	4052	}
3667		4053
3668	#if EV_PERIODIC_ENABLE	4054	#if EV_PERIODIC_ENABLE
3669	void noinline	4055	ecb_noinline
		4056	void
3670	ev_periodic_start (EV_P_ ev_periodic *w) EV_THROW	4057	ev_periodic_start (EV_P_ ev_periodic *w) EV_NOEXCEPT
3671	{	4058	{
3672	if (expect_false (ev_is_active (w)))	4059	if (ecb_expect_false (ev_is_active (w)))
3673	return;	4060	return;
3674		4061
3675	if (w->reschedule_cb)	4062	if (w->reschedule_cb)
3676	ev_at (w) = w->reschedule_cb (w, ev_rt_now);	4063	ev_at (w) = w->reschedule_cb (w, ev_rt_now);
3677	else if (w->interval)	4064	else if (w->interval)
…		…
3684		4071
3685	EV_FREQUENT_CHECK;	4072	EV_FREQUENT_CHECK;
3686		4073
3687	++periodiccnt;	4074	++periodiccnt;
3688	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);	4075	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);
3689	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, EMPTY2);	4076	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, array_needsize_noinit);
3690	ANHE_w (periodics [ev_active (w)]) = (WT)w;	4077	ANHE_w (periodics [ev_active (w)]) = (WT)w;
3691	ANHE_at_cache (periodics [ev_active (w)]);	4078	ANHE_at_cache (periodics [ev_active (w)]);
3692	upheap (periodics, ev_active (w));	4079	upheap (periodics, ev_active (w));
3693		4080
3694	EV_FREQUENT_CHECK;	4081	EV_FREQUENT_CHECK;
3695		4082
3696	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/	4083	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/
3697	}	4084	}
3698		4085
3699	void noinline	4086	ecb_noinline
		4087	void
3700	ev_periodic_stop (EV_P_ ev_periodic *w) EV_THROW	4088	ev_periodic_stop (EV_P_ ev_periodic *w) EV_NOEXCEPT
3701	{	4089	{
3702	clear_pending (EV_A_ (W)w);	4090	clear_pending (EV_A_ (W)w);
3703	if (expect_false (!ev_is_active (w)))	4091	if (ecb_expect_false (!ev_is_active (w)))
3704	return;	4092	return;
3705		4093
3706	EV_FREQUENT_CHECK;	4094	EV_FREQUENT_CHECK;
3707		4095
3708	{	4096	{
…		…
3710		4098
3711	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));	4099	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));
3712		4100
3713	--periodiccnt;	4101	--periodiccnt;
3714		4102
3715	if (expect_true (active < periodiccnt + HEAP0))	4103	if (ecb_expect_true (active < periodiccnt + HEAP0))
3716	{	4104	{
3717	periodics [active] = periodics [periodiccnt + HEAP0];	4105	periodics [active] = periodics [periodiccnt + HEAP0];
3718	adjustheap (periodics, periodiccnt, active);	4106	adjustheap (periodics, periodiccnt, active);
3719	}	4107	}
3720	}	4108	}
…		…
3722	ev_stop (EV_A_ (W)w);	4110	ev_stop (EV_A_ (W)w);
3723		4111
3724	EV_FREQUENT_CHECK;	4112	EV_FREQUENT_CHECK;
3725	}	4113	}
3726		4114
3727	void noinline	4115	ecb_noinline
		4116	void
3728	ev_periodic_again (EV_P_ ev_periodic *w) EV_THROW	4117	ev_periodic_again (EV_P_ ev_periodic *w) EV_NOEXCEPT
3729	{	4118	{
3730	/* TODO: use adjustheap and recalculation */	4119	/* TODO: use adjustheap and recalculation */
3731	ev_periodic_stop (EV_A_ w);	4120	ev_periodic_stop (EV_A_ w);
3732	ev_periodic_start (EV_A_ w);	4121	ev_periodic_start (EV_A_ w);
3733	}	4122	}
…		…
3737	# define SA_RESTART 0	4126	# define SA_RESTART 0
3738	#endif	4127	#endif
3739		4128
3740	#if EV_SIGNAL_ENABLE	4129	#if EV_SIGNAL_ENABLE
3741		4130
3742	void noinline	4131	ecb_noinline
		4132	void
3743	ev_signal_start (EV_P_ ev_signal *w) EV_THROW	4133	ev_signal_start (EV_P_ ev_signal *w) EV_NOEXCEPT
3744	{	4134	{
3745	if (expect_false (ev_is_active (w)))	4135	if (ecb_expect_false (ev_is_active (w)))
3746	return;	4136	return;
3747		4137
3748	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));	4138	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));
3749		4139
3750	#if EV_MULTIPLICITY	4140	#if EV_MULTIPLICITY
…		…
3819	}	4209	}
3820		4210
3821	EV_FREQUENT_CHECK;	4211	EV_FREQUENT_CHECK;
3822	}	4212	}
3823		4213
3824	void noinline	4214	ecb_noinline
		4215	void
3825	ev_signal_stop (EV_P_ ev_signal *w) EV_THROW	4216	ev_signal_stop (EV_P_ ev_signal *w) EV_NOEXCEPT
3826	{	4217	{
3827	clear_pending (EV_A_ (W)w);	4218	clear_pending (EV_A_ (W)w);
3828	if (expect_false (!ev_is_active (w)))	4219	if (ecb_expect_false (!ev_is_active (w)))
3829	return;	4220	return;
3830		4221
3831	EV_FREQUENT_CHECK;	4222	EV_FREQUENT_CHECK;
3832		4223
3833	wlist_del (&signals [w->signum - 1].head, (WL)w);	4224	wlist_del (&signals [w->signum - 1].head, (WL)w);
…		…
3861	#endif	4252	#endif
3862		4253
3863	#if EV_CHILD_ENABLE	4254	#if EV_CHILD_ENABLE
3864		4255
3865	void	4256	void
3866	ev_child_start (EV_P_ ev_child *w) EV_THROW	4257	ev_child_start (EV_P_ ev_child *w) EV_NOEXCEPT
3867	{	4258	{
3868	#if EV_MULTIPLICITY	4259	#if EV_MULTIPLICITY
3869	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));	4260	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));
3870	#endif	4261	#endif
3871	if (expect_false (ev_is_active (w)))	4262	if (ecb_expect_false (ev_is_active (w)))
3872	return;	4263	return;
3873		4264
3874	EV_FREQUENT_CHECK;	4265	EV_FREQUENT_CHECK;
3875		4266
3876	ev_start (EV_A_ (W)w, 1);	4267	ev_start (EV_A_ (W)w, 1);
…		…
3878		4269
3879	EV_FREQUENT_CHECK;	4270	EV_FREQUENT_CHECK;
3880	}	4271	}
3881		4272
3882	void	4273	void
3883	ev_child_stop (EV_P_ ev_child *w) EV_THROW	4274	ev_child_stop (EV_P_ ev_child *w) EV_NOEXCEPT
3884	{	4275	{
3885	clear_pending (EV_A_ (W)w);	4276	clear_pending (EV_A_ (W)w);
3886	if (expect_false (!ev_is_active (w)))	4277	if (ecb_expect_false (!ev_is_active (w)))
3887	return;	4278	return;
3888		4279
3889	EV_FREQUENT_CHECK;	4280	EV_FREQUENT_CHECK;
3890		4281
3891	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);	4282	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);
…		…
3905		4296
3906	#define DEF_STAT_INTERVAL 5.0074891	4297	#define DEF_STAT_INTERVAL 5.0074891
3907	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */	4298	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */
3908	#define MIN_STAT_INTERVAL 0.1074891	4299	#define MIN_STAT_INTERVAL 0.1074891
3909		4300
3910	static void noinline stat_timer_cb (EV_P_ ev_timer *w_, int revents);	4301	ecb_noinline static void stat_timer_cb (EV_P_ ev_timer *w_, int revents);
3911		4302
3912	#if EV_USE_INOTIFY	4303	#if EV_USE_INOTIFY
3913		4304
3914	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */	4305	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */
3915	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)	4306	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)
3916		4307
3917	static void noinline	4308	ecb_noinline
		4309	static void
3918	infy_add (EV_P_ ev_stat *w)	4310	infy_add (EV_P_ ev_stat *w)
3919	{	4311	{
3920	w->wd = inotify_add_watch (fs_fd, w->path,	4312	w->wd = inotify_add_watch (fs_fd, w->path,
3921	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY	4313	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY
3922	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO	4314	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO
…		…
3986	if (ev_is_active (&w->timer)) ev_ref (EV_A);	4378	if (ev_is_active (&w->timer)) ev_ref (EV_A);
3987	ev_timer_again (EV_A_ &w->timer);	4379	ev_timer_again (EV_A_ &w->timer);
3988	if (ev_is_active (&w->timer)) ev_unref (EV_A);	4380	if (ev_is_active (&w->timer)) ev_unref (EV_A);
3989	}	4381	}
3990		4382
3991	static void noinline	4383	ecb_noinline
		4384	static void
3992	infy_del (EV_P_ ev_stat *w)	4385	infy_del (EV_P_ ev_stat *w)
3993	{	4386	{
3994	int slot;	4387	int slot;
3995	int wd = w->wd;	4388	int wd = w->wd;
3996		4389
…		…
4003		4396
4004	/* remove this watcher, if others are watching it, they will rearm */	4397	/* remove this watcher, if others are watching it, they will rearm */
4005	inotify_rm_watch (fs_fd, wd);	4398	inotify_rm_watch (fs_fd, wd);
4006	}	4399	}
4007		4400
4008	static void noinline	4401	ecb_noinline
		4402	static void
4009	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)	4403	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)
4010	{	4404	{
4011	if (slot < 0)	4405	if (slot < 0)
4012	/* overflow, need to check for all hash slots */	4406	/* overflow, need to check for all hash slots */
4013	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)	4407	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)
…		…
4049	infy_wd (EV_A_ ev->wd, ev->wd, ev);	4443	infy_wd (EV_A_ ev->wd, ev->wd, ev);
4050	ofs += sizeof (struct inotify_event) + ev->len;	4444	ofs += sizeof (struct inotify_event) + ev->len;
4051	}	4445	}
4052	}	4446	}
4053		4447
4054	inline_size void ecb_cold	4448	inline_size ecb_cold
		4449	void
4055	ev_check_2625 (EV_P)	4450	ev_check_2625 (EV_P)
4056	{	4451	{
4057	/* kernels < 2.6.25 are borked	4452	/* kernels < 2.6.25 are borked
4058	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html	4453	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html
4059	*/	4454	*/
…		…
4149	#else	4544	#else
4150	# define EV_LSTAT(p,b) lstat (p, b)	4545	# define EV_LSTAT(p,b) lstat (p, b)
4151	#endif	4546	#endif
4152		4547
4153	void	4548	void
4154	ev_stat_stat (EV_P_ ev_stat *w) EV_THROW	4549	ev_stat_stat (EV_P_ ev_stat *w) EV_NOEXCEPT
4155	{	4550	{
4156	if (lstat (w->path, &w->attr) < 0)	4551	if (lstat (w->path, &w->attr) < 0)
4157	w->attr.st_nlink = 0;	4552	w->attr.st_nlink = 0;
4158	else if (!w->attr.st_nlink)	4553	else if (!w->attr.st_nlink)
4159	w->attr.st_nlink = 1;	4554	w->attr.st_nlink = 1;
4160	}	4555	}
4161		4556
4162	static void noinline	4557	ecb_noinline
		4558	static void
4163	stat_timer_cb (EV_P_ ev_timer *w_, int revents)	4559	stat_timer_cb (EV_P_ ev_timer *w_, int revents)
4164	{	4560	{
4165	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));	4561	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));
4166		4562
4167	ev_statdata prev = w->attr;	4563	ev_statdata prev = w->attr;
…		…
4198	ev_feed_event (EV_A_ w, EV_STAT);	4594	ev_feed_event (EV_A_ w, EV_STAT);
4199	}	4595	}
4200	}	4596	}
4201		4597
4202	void	4598	void
4203	ev_stat_start (EV_P_ ev_stat *w) EV_THROW	4599	ev_stat_start (EV_P_ ev_stat *w) EV_NOEXCEPT
4204	{	4600	{
4205	if (expect_false (ev_is_active (w)))	4601	if (ecb_expect_false (ev_is_active (w)))
4206	return;	4602	return;
4207		4603
4208	ev_stat_stat (EV_A_ w);	4604	ev_stat_stat (EV_A_ w);
4209		4605
4210	if (w->interval < MIN_STAT_INTERVAL && w->interval)	4606	if (w->interval < MIN_STAT_INTERVAL && w->interval)
…		…
4229		4625
4230	EV_FREQUENT_CHECK;	4626	EV_FREQUENT_CHECK;
4231	}	4627	}
4232		4628
4233	void	4629	void
4234	ev_stat_stop (EV_P_ ev_stat *w) EV_THROW	4630	ev_stat_stop (EV_P_ ev_stat *w) EV_NOEXCEPT
4235	{	4631	{
4236	clear_pending (EV_A_ (W)w);	4632	clear_pending (EV_A_ (W)w);
4237	if (expect_false (!ev_is_active (w)))	4633	if (ecb_expect_false (!ev_is_active (w)))
4238	return;	4634	return;
4239		4635
4240	EV_FREQUENT_CHECK;	4636	EV_FREQUENT_CHECK;
4241		4637
4242	#if EV_USE_INOTIFY	4638	#if EV_USE_INOTIFY
…		…
4255	}	4651	}
4256	#endif	4652	#endif
4257		4653
4258	#if EV_IDLE_ENABLE	4654	#if EV_IDLE_ENABLE
4259	void	4655	void
4260	ev_idle_start (EV_P_ ev_idle *w) EV_THROW	4656	ev_idle_start (EV_P_ ev_idle *w) EV_NOEXCEPT
4261	{	4657	{
4262	if (expect_false (ev_is_active (w)))	4658	if (ecb_expect_false (ev_is_active (w)))
4263	return;	4659	return;
4264		4660
4265	pri_adjust (EV_A_ (W)w);	4661	pri_adjust (EV_A_ (W)w);
4266		4662
4267	EV_FREQUENT_CHECK;	4663	EV_FREQUENT_CHECK;
…		…
4270	int active = ++idlecnt [ABSPRI (w)];	4666	int active = ++idlecnt [ABSPRI (w)];
4271		4667
4272	++idleall;	4668	++idleall;
4273	ev_start (EV_A_ (W)w, active);	4669	ev_start (EV_A_ (W)w, active);
4274		4670
4275	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, EMPTY2);	4671	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, array_needsize_noinit);
4276	idles [ABSPRI (w)][active - 1] = w;	4672	idles [ABSPRI (w)][active - 1] = w;
4277	}	4673	}
4278		4674
4279	EV_FREQUENT_CHECK;	4675	EV_FREQUENT_CHECK;
4280	}	4676	}
4281		4677
4282	void	4678	void
4283	ev_idle_stop (EV_P_ ev_idle *w) EV_THROW	4679	ev_idle_stop (EV_P_ ev_idle *w) EV_NOEXCEPT
4284	{	4680	{
4285	clear_pending (EV_A_ (W)w);	4681	clear_pending (EV_A_ (W)w);
4286	if (expect_false (!ev_is_active (w)))	4682	if (ecb_expect_false (!ev_is_active (w)))
4287	return;	4683	return;
4288		4684
4289	EV_FREQUENT_CHECK;	4685	EV_FREQUENT_CHECK;
4290		4686
4291	{	4687	{
…		…
4302	}	4698	}
4303	#endif	4699	#endif
4304		4700
4305	#if EV_PREPARE_ENABLE	4701	#if EV_PREPARE_ENABLE
4306	void	4702	void
4307	ev_prepare_start (EV_P_ ev_prepare *w) EV_THROW	4703	ev_prepare_start (EV_P_ ev_prepare *w) EV_NOEXCEPT
4308	{	4704	{
4309	if (expect_false (ev_is_active (w)))	4705	if (ecb_expect_false (ev_is_active (w)))
4310	return;	4706	return;
4311		4707
4312	EV_FREQUENT_CHECK;	4708	EV_FREQUENT_CHECK;
4313		4709
4314	ev_start (EV_A_ (W)w, ++preparecnt);	4710	ev_start (EV_A_ (W)w, ++preparecnt);
4315	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, EMPTY2);	4711	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, array_needsize_noinit);
4316	prepares [preparecnt - 1] = w;	4712	prepares [preparecnt - 1] = w;
4317		4713
4318	EV_FREQUENT_CHECK;	4714	EV_FREQUENT_CHECK;
4319	}	4715	}
4320		4716
4321	void	4717	void
4322	ev_prepare_stop (EV_P_ ev_prepare *w) EV_THROW	4718	ev_prepare_stop (EV_P_ ev_prepare *w) EV_NOEXCEPT
4323	{	4719	{
4324	clear_pending (EV_A_ (W)w);	4720	clear_pending (EV_A_ (W)w);
4325	if (expect_false (!ev_is_active (w)))	4721	if (ecb_expect_false (!ev_is_active (w)))
4326	return;	4722	return;
4327		4723
4328	EV_FREQUENT_CHECK;	4724	EV_FREQUENT_CHECK;
4329		4725
4330	{	4726	{
…		…
4340	}	4736	}
4341	#endif	4737	#endif
4342		4738
4343	#if EV_CHECK_ENABLE	4739	#if EV_CHECK_ENABLE
4344	void	4740	void
4345	ev_check_start (EV_P_ ev_check *w) EV_THROW	4741	ev_check_start (EV_P_ ev_check *w) EV_NOEXCEPT
4346	{	4742	{
4347	if (expect_false (ev_is_active (w)))	4743	if (ecb_expect_false (ev_is_active (w)))
4348	return;	4744	return;
4349		4745
4350	EV_FREQUENT_CHECK;	4746	EV_FREQUENT_CHECK;
4351		4747
4352	ev_start (EV_A_ (W)w, ++checkcnt);	4748	ev_start (EV_A_ (W)w, ++checkcnt);
4353	array_needsize (ev_check *, checks, checkmax, checkcnt, EMPTY2);	4749	array_needsize (ev_check *, checks, checkmax, checkcnt, array_needsize_noinit);
4354	checks [checkcnt - 1] = w;	4750	checks [checkcnt - 1] = w;
4355		4751
4356	EV_FREQUENT_CHECK;	4752	EV_FREQUENT_CHECK;
4357	}	4753	}
4358		4754
4359	void	4755	void
4360	ev_check_stop (EV_P_ ev_check *w) EV_THROW	4756	ev_check_stop (EV_P_ ev_check *w) EV_NOEXCEPT
4361	{	4757	{
4362	clear_pending (EV_A_ (W)w);	4758	clear_pending (EV_A_ (W)w);
4363	if (expect_false (!ev_is_active (w)))	4759	if (ecb_expect_false (!ev_is_active (w)))
4364	return;	4760	return;
4365		4761
4366	EV_FREQUENT_CHECK;	4762	EV_FREQUENT_CHECK;
4367		4763
4368	{	4764	{
…		…
4377	EV_FREQUENT_CHECK;	4773	EV_FREQUENT_CHECK;
4378	}	4774	}
4379	#endif	4775	#endif
4380		4776
4381	#if EV_EMBED_ENABLE	4777	#if EV_EMBED_ENABLE
4382	void noinline	4778	ecb_noinline
		4779	void
4383	ev_embed_sweep (EV_P_ ev_embed *w) EV_THROW	4780	ev_embed_sweep (EV_P_ ev_embed *w) EV_NOEXCEPT
4384	{	4781	{
4385	ev_run (w->other, EVRUN_NOWAIT);	4782	ev_run (w->other, EVRUN_NOWAIT);
4386	}	4783	}
4387		4784
4388	static void	4785	static void
…		…
4436	ev_idle_stop (EV_A_ idle);	4833	ev_idle_stop (EV_A_ idle);
4437	}	4834	}
4438	#endif	4835	#endif
4439		4836
4440	void	4837	void
4441	ev_embed_start (EV_P_ ev_embed *w) EV_THROW	4838	ev_embed_start (EV_P_ ev_embed *w) EV_NOEXCEPT
4442	{	4839	{
4443	if (expect_false (ev_is_active (w)))	4840	if (ecb_expect_false (ev_is_active (w)))
4444	return;	4841	return;
4445		4842
4446	{	4843	{
4447	EV_P = w->other;	4844	EV_P = w->other;
4448	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));	4845	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));
…		…
4467		4864
4468	EV_FREQUENT_CHECK;	4865	EV_FREQUENT_CHECK;
4469	}	4866	}
4470		4867
4471	void	4868	void
4472	ev_embed_stop (EV_P_ ev_embed *w) EV_THROW	4869	ev_embed_stop (EV_P_ ev_embed *w) EV_NOEXCEPT
4473	{	4870	{
4474	clear_pending (EV_A_ (W)w);	4871	clear_pending (EV_A_ (W)w);
4475	if (expect_false (!ev_is_active (w)))	4872	if (ecb_expect_false (!ev_is_active (w)))
4476	return;	4873	return;
4477		4874
4478	EV_FREQUENT_CHECK;	4875	EV_FREQUENT_CHECK;
4479		4876
4480	ev_io_stop (EV_A_ &w->io);	4877	ev_io_stop (EV_A_ &w->io);
…		…
4487	}	4884	}
4488	#endif	4885	#endif
4489		4886
4490	#if EV_FORK_ENABLE	4887	#if EV_FORK_ENABLE
4491	void	4888	void
4492	ev_fork_start (EV_P_ ev_fork *w) EV_THROW	4889	ev_fork_start (EV_P_ ev_fork *w) EV_NOEXCEPT
4493	{	4890	{
4494	if (expect_false (ev_is_active (w)))	4891	if (ecb_expect_false (ev_is_active (w)))
4495	return;	4892	return;
4496		4893
4497	EV_FREQUENT_CHECK;	4894	EV_FREQUENT_CHECK;
4498		4895
4499	ev_start (EV_A_ (W)w, ++forkcnt);	4896	ev_start (EV_A_ (W)w, ++forkcnt);
4500	array_needsize (ev_fork *, forks, forkmax, forkcnt, EMPTY2);	4897	array_needsize (ev_fork *, forks, forkmax, forkcnt, array_needsize_noinit);
4501	forks [forkcnt - 1] = w;	4898	forks [forkcnt - 1] = w;
4502		4899
4503	EV_FREQUENT_CHECK;	4900	EV_FREQUENT_CHECK;
4504	}	4901	}
4505		4902
4506	void	4903	void
4507	ev_fork_stop (EV_P_ ev_fork *w) EV_THROW	4904	ev_fork_stop (EV_P_ ev_fork *w) EV_NOEXCEPT
4508	{	4905	{
4509	clear_pending (EV_A_ (W)w);	4906	clear_pending (EV_A_ (W)w);
4510	if (expect_false (!ev_is_active (w)))	4907	if (ecb_expect_false (!ev_is_active (w)))
4511	return;	4908	return;
4512		4909
4513	EV_FREQUENT_CHECK;	4910	EV_FREQUENT_CHECK;
4514		4911
4515	{	4912	{
…		…
4525	}	4922	}
4526	#endif	4923	#endif
4527		4924
4528	#if EV_CLEANUP_ENABLE	4925	#if EV_CLEANUP_ENABLE
4529	void	4926	void
4530	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_THROW	4927	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4531	{	4928	{
4532	if (expect_false (ev_is_active (w)))	4929	if (ecb_expect_false (ev_is_active (w)))
4533	return;	4930	return;
4534		4931
4535	EV_FREQUENT_CHECK;	4932	EV_FREQUENT_CHECK;
4536		4933
4537	ev_start (EV_A_ (W)w, ++cleanupcnt);	4934	ev_start (EV_A_ (W)w, ++cleanupcnt);
4538	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, EMPTY2);	4935	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, array_needsize_noinit);
4539	cleanups [cleanupcnt - 1] = w;	4936	cleanups [cleanupcnt - 1] = w;
4540		4937
4541	/* cleanup watchers should never keep a refcount on the loop */	4938	/* cleanup watchers should never keep a refcount on the loop */
4542	ev_unref (EV_A);	4939	ev_unref (EV_A);
4543	EV_FREQUENT_CHECK;	4940	EV_FREQUENT_CHECK;
4544	}	4941	}
4545		4942
4546	void	4943	void
4547	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_THROW	4944	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4548	{	4945	{
4549	clear_pending (EV_A_ (W)w);	4946	clear_pending (EV_A_ (W)w);
4550	if (expect_false (!ev_is_active (w)))	4947	if (ecb_expect_false (!ev_is_active (w)))
4551	return;	4948	return;
4552		4949
4553	EV_FREQUENT_CHECK;	4950	EV_FREQUENT_CHECK;
4554	ev_ref (EV_A);	4951	ev_ref (EV_A);
4555		4952
…		…
4566	}	4963	}
4567	#endif	4964	#endif
4568		4965
4569	#if EV_ASYNC_ENABLE	4966	#if EV_ASYNC_ENABLE
4570	void	4967	void
4571	ev_async_start (EV_P_ ev_async *w) EV_THROW	4968	ev_async_start (EV_P_ ev_async *w) EV_NOEXCEPT
4572	{	4969	{
4573	if (expect_false (ev_is_active (w)))	4970	if (ecb_expect_false (ev_is_active (w)))
4574	return;	4971	return;
4575		4972
4576	w->sent = 0;	4973	w->sent = 0;
4577		4974
4578	evpipe_init (EV_A);	4975	evpipe_init (EV_A);
4579		4976
4580	EV_FREQUENT_CHECK;	4977	EV_FREQUENT_CHECK;
4581		4978
4582	ev_start (EV_A_ (W)w, ++asynccnt);	4979	ev_start (EV_A_ (W)w, ++asynccnt);
4583	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, EMPTY2);	4980	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, array_needsize_noinit);
4584	asyncs [asynccnt - 1] = w;	4981	asyncs [asynccnt - 1] = w;
4585		4982
4586	EV_FREQUENT_CHECK;	4983	EV_FREQUENT_CHECK;
4587	}	4984	}
4588		4985
4589	void	4986	void
4590	ev_async_stop (EV_P_ ev_async *w) EV_THROW	4987	ev_async_stop (EV_P_ ev_async *w) EV_NOEXCEPT
4591	{	4988	{
4592	clear_pending (EV_A_ (W)w);	4989	clear_pending (EV_A_ (W)w);
4593	if (expect_false (!ev_is_active (w)))	4990	if (ecb_expect_false (!ev_is_active (w)))
4594	return;	4991	return;
4595		4992
4596	EV_FREQUENT_CHECK;	4993	EV_FREQUENT_CHECK;
4597		4994
4598	{	4995	{
…		…
4606		5003
4607	EV_FREQUENT_CHECK;	5004	EV_FREQUENT_CHECK;
4608	}	5005	}
4609		5006
4610	void	5007	void
4611	ev_async_send (EV_P_ ev_async *w) EV_THROW	5008	ev_async_send (EV_P_ ev_async *w) EV_NOEXCEPT
4612	{	5009	{
4613	w->sent = 1;	5010	w->sent = 1;
4614	evpipe_write (EV_A_ &async_pending);	5011	evpipe_write (EV_A_ &async_pending);
4615	}	5012	}
4616	#endif	5013	#endif
…		…
4653		5050
4654	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));	5051	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));
4655	}	5052	}
4656		5053
4657	void	5054	void
4658	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_THROW	5055	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_NOEXCEPT
4659	{	5056	{
4660	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));	5057	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));
4661
4662	if (expect_false (!once))
4663	{
4664	cb (EV_ERROR | EV_READ | EV_WRITE | EV_TIMER, arg);
4665	return;
4666	}
4667		5058
4668	once->cb = cb;	5059	once->cb = cb;
4669	once->arg = arg;	5060	once->arg = arg;
4670		5061
4671	ev_init (&once->io, once_cb_io);	5062	ev_init (&once->io, once_cb_io);
…		…
4684	}	5075	}
4685		5076
4686	/*****************************************************************************/	5077	/*****************************************************************************/
4687		5078
4688	#if EV_WALK_ENABLE	5079	#if EV_WALK_ENABLE
4689	void ecb_cold	5080	ecb_cold
		5081	void
4690	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_THROW	5082	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_NOEXCEPT
4691	{	5083	{
4692	int i, j;	5084	int i, j;
4693	ev_watcher_list *wl, *wn;	5085	ev_watcher_list *wl, *wn;
4694		5086
4695	if (types & (EV_IO | EV_EMBED))	5087	if (types & (EV_IO | EV_EMBED))

Diff Legend

–	Removed lines
+	Added lines
<	Changed lines
>	Changed lines