ViewVC Help

View File | Revision Log | Show Annotations | Download File

/cvs/libev/ev.c

Comparing libev/ev.c (file contents):
Revision 1.458 by root, Sun Oct 27 16:26:07 2013 UTC vs.
Revision 1.507 by root, Thu Jul 11 08:22:54 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
		337	#ifndef EV_USE_IOURING
		338	# if __linux
		339	# define EV_USE_IOURING 0
		340	# else
		341	# define EV_USE_IOURING 0
		342	# endif
		343	#endif
		344
312	#ifndef EV_USE_INOTIFY	345	#ifndef EV_USE_INOTIFY
313	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))	346	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))
314	# define EV_USE_INOTIFY EV_FEATURE_OS	347	# define EV_USE_INOTIFY EV_FEATURE_OS
315	# else	348	# else
316	# define EV_USE_INOTIFY 0	349	# define EV_USE_INOTIFY 0
…		…
357		390
358	#ifndef EV_HEAP_CACHE_AT	391	#ifndef EV_HEAP_CACHE_AT
359	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA	392	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA
360	#endif	393	#endif
361		394
362	#ifdef ANDROID	395	#ifdef __ANDROID__
363	/* supposedly, android doesn't typedef fd_mask */	396	/* supposedly, android doesn't typedef fd_mask */
364	# undef EV_USE_SELECT	397	# undef EV_USE_SELECT
365	# define EV_USE_SELECT 0	398	# define EV_USE_SELECT 0
366	/* supposedly, we need to include syscall.h, not sys/syscall.h, so just disable */	399	/* supposedly, we need to include syscall.h, not sys/syscall.h, so just disable */
367	# undef EV_USE_CLOCK_SYSCALL	400	# undef EV_USE_CLOCK_SYSCALL
…		…
381	# include <sys/syscall.h>	414	# include <sys/syscall.h>
382	# ifdef SYS_clock_gettime	415	# ifdef SYS_clock_gettime
383	# define clock_gettime(id, ts) syscall (SYS_clock_gettime, (id), (ts))	416	# define clock_gettime(id, ts) syscall (SYS_clock_gettime, (id), (ts))
384	# undef EV_USE_MONOTONIC	417	# undef EV_USE_MONOTONIC
385	# define EV_USE_MONOTONIC 1	418	# define EV_USE_MONOTONIC 1
		419	# define EV_NEED_SYSCALL 1
386	# else	420	# else
387	# undef EV_USE_CLOCK_SYSCALL	421	# undef EV_USE_CLOCK_SYSCALL
388	# define EV_USE_CLOCK_SYSCALL 0	422	# define EV_USE_CLOCK_SYSCALL 0
389	# endif	423	# endif
390	#endif	424	#endif
…		…
408		442
409	#if !EV_USE_NANOSLEEP	443	#if !EV_USE_NANOSLEEP
410	/* hp-ux has it in sys/time.h, which we unconditionally include above */	444	/* hp-ux has it in sys/time.h, which we unconditionally include above */
411	# if !defined _WIN32 && !defined __hpux	445	# if !defined _WIN32 && !defined __hpux
412	# include <sys/select.h>	446	# include <sys/select.h>
		447	# endif
		448	#endif
		449
		450	#if EV_USE_LINUXAIO
		451	# include <sys/syscall.h>
		452	# if SYS_io_getevents && EV_USE_EPOLL /* linuxaio backend requires epoll backend */
		453	# define EV_NEED_SYSCALL 1
		454	# else
		455	# undef EV_USE_LINUXAIO
		456	# define EV_USE_LINUXAIO 0
		457	# endif
		458	#endif
		459
		460	#if EV_USE_IOURING
		461	# include <sys/syscall.h>
		462	# if !SYS_io_uring_setup && __linux && !__alpha
		463	# define SYS_io_uring_setup 425
		464	# define SYS_io_uring_enter 426
		465	# define SYS_io_uring_wregister 427
		466	# endif
		467	# if SYS_io_uring_setup && EV_USE_EPOLL /* iouring backend requires epoll backend */
		468	# define EV_NEED_SYSCALL 1
		469	# else
		470	# undef EV_USE_IOURING
		471	# define EV_USE_IOURING 0
413	# endif	472	# endif
414	#endif	473	#endif
415		474
416	#if EV_USE_INOTIFY	475	#if EV_USE_INOTIFY
417	# include <sys/statfs.h>	476	# include <sys/statfs.h>
…		…
459	uint32_t ssi_signo;	518	uint32_t ssi_signo;
460	char pad[128 - sizeof (uint32_t)];	519	char pad[128 - sizeof (uint32_t)];
461	};	520	};
462	#endif	521	#endif
463		522
464	/**/	523	/*****************************************************************************/
465		524
466	#if EV_VERIFY >= 3	525	#if EV_VERIFY >= 3
467	# define EV_FREQUENT_CHECK ev_verify (EV_A)	526	# define EV_FREQUENT_CHECK ev_verify (EV_A)
468	#else	527	#else
469	# define EV_FREQUENT_CHECK do { } while (0)	528	# define EV_FREQUENT_CHECK do { } while (0)
…		…
474	* This value is good at least till the year 4000.	533	* This value is good at least till the year 4000.
475	*/	534	*/
476	#define MIN_INTERVAL 0.0001220703125 /* 1/2**13, good till 4000 */	535	#define MIN_INTERVAL 0.0001220703125 /* 1/2**13, good till 4000 */
477	/*#define MIN_INTERVAL 0.00000095367431640625 /* 1/2**20, good till 2200 */	536	/*#define MIN_INTERVAL 0.00000095367431640625 /* 1/2**20, good till 2200 */
478		537
479	#define MIN_TIMEJUMP 1. /* minimum timejump that gets detected (if monotonic clock available) */	538	#define MIN_TIMEJUMP 1. /* minimum timejump that gets detected (if monotonic clock available) */
480	#define MAX_BLOCKTIME 59.743 /* never wait longer than this time (to detect time jumps) */	539	#define MAX_BLOCKTIME 59.743 /* never wait longer than this time (to detect time jumps) */
481		540
		541	/* find a portable timestamp that is "always" in the future but fits into time_t.
		542	* this is quite hard, and we are mostly guessing - we handle 32 bit signed/unsigned time_t,
		543	* and sizes larger than 32 bit, and maybe the unlikely floating point time_t */
		544	#define EV_TSTAMP_HUGE \
		545	(sizeof (time_t) >= 8 ? 10000000000000. \
		546	: 0 < (time_t)4294967295 ? 4294967295. \
		547	: 2147483647.) \
		548
		549	#define EV_TS_TO_MS(a) a * 1e3 + 0.9999
		550	#define EV_TS_FROM_USEC(us) us * 1e-6
482	#define EV_TV_SET(tv,t) do { tv.tv_sec = (long)t; tv.tv_usec = (long)((t - tv.tv_sec) * 1e6); } while (0)	551	#define EV_TV_SET(tv,t) do { tv.tv_sec = (long)t; tv.tv_usec = (long)((t - tv.tv_sec) * 1e6); } while (0)
483	#define EV_TS_SET(ts,t) do { ts.tv_sec = (long)t; ts.tv_nsec = (long)((t - ts.tv_sec) * 1e9); } while (0)	552	#define EV_TS_SET(ts,t) do { ts.tv_sec = (long)t; ts.tv_nsec = (long)((t - ts.tv_sec) * 1e9); } while (0)
		553	#define EV_TV_GET(tv) ((tv).tv_sec + (tv).tv_usec * 1e-6)
		554	#define EV_TS_GET(ts) ((ts).tv_sec + (ts).tv_nsec * 1e-9)
484		555
485	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */	556	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */
486	/* ECB.H BEGIN */	557	/* ECB.H BEGIN */
487	/*	558	/*
488	* libecb - http://software.schmorp.de/pkg/libecb	559	* libecb - http://software.schmorp.de/pkg/libecb
489	*	560	*
490	* Copyright (©) 2009-2012 Marc Alexander Lehmann <libecb@schmorp.de>	561	* Copyright (©) 2009-2015 Marc Alexander Lehmann <libecb@schmorp.de>
491	* Copyright (©) 2011 Emanuele Giaquinta	562	* Copyright (©) 2011 Emanuele Giaquinta
492	* All rights reserved.	563	* All rights reserved.
493	*	564	*
494	* Redistribution and use in source and binary forms, with or without modifica-	565	* Redistribution and use in source and binary forms, with or without modifica-
495	* tion, are permitted provided that the following conditions are met:	566	* tion, are permitted provided that the following conditions are met:
…		…
509	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;	580	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;
510	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,	581	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,
511	* WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING NEGLIGENCE OR OTH-	582	* 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	583	* ERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED
513	* OF THE POSSIBILITY OF SUCH DAMAGE.	584	* OF THE POSSIBILITY OF SUCH DAMAGE.
		585	*
		586	* Alternatively, the contents of this file may be used under the terms of
		587	* the GNU General Public License ("GPL") version 2 or any later version,
		588	* in which case the provisions of the GPL are applicable instead of
		589	* the above. If you wish to allow the use of your version of this file
		590	* only under the terms of the GPL and not to allow others to use your
		591	* version of this file under the BSD license, indicate your decision
		592	* by deleting the provisions above and replace them with the notice
		593	* and other provisions required by the GPL. If you do not delete the
		594	* provisions above, a recipient may use your version of this file under
		595	* either the BSD or the GPL.
514	*/	596	*/
515		597
516	#ifndef ECB_H	598	#ifndef ECB_H
517	#define ECB_H	599	#define ECB_H
518		600
519	/* 16 bits major, 16 bits minor */	601	/* 16 bits major, 16 bits minor */
520	#define ECB_VERSION 0x00010003	602	#define ECB_VERSION 0x00010006
521		603
522	#ifdef _WIN32	604	#ifdef _WIN32
523	typedef signed char int8_t;	605	typedef signed char int8_t;
524	typedef unsigned char uint8_t;	606	typedef unsigned char uint8_t;
525	typedef signed short int16_t;	607	typedef signed short int16_t;
…		…
542	typedef uint32_t uintptr_t;	624	typedef uint32_t uintptr_t;
543	typedef int32_t intptr_t;	625	typedef int32_t intptr_t;
544	#endif	626	#endif
545	#else	627	#else
546	#include <inttypes.h>	628	#include <inttypes.h>
547	#if UINTMAX_MAX > 0xffffffffU	629	#if (defined INTPTR_MAX ? INTPTR_MAX : ULONG_MAX) > 0xffffffffU
548	#define ECB_PTRSIZE 8	630	#define ECB_PTRSIZE 8
549	#else	631	#else
550	#define ECB_PTRSIZE 4	632	#define ECB_PTRSIZE 4
551	#endif	633	#endif
552	#endif	634	#endif
553		635
		636	#define ECB_GCC_AMD64 (__amd64 || __amd64__ || __x86_64 || __x86_64__)
		637	#define ECB_MSVC_AMD64 (_M_AMD64 || _M_X64)
		638
554	/* work around x32 idiocy by defining proper macros */	639	/* work around x32 idiocy by defining proper macros */
555	#if __x86_64 || _M_AMD64	640	#if ECB_GCC_AMD64 || ECB_MSVC_AMD64
556	#if _ILP32	641	#if _ILP32
557	#define ECB_AMD64_X32 1	642	#define ECB_AMD64_X32 1
558	#else	643	#else
559	#define ECB_AMD64 1	644	#define ECB_AMD64 1
560	#endif	645	#endif
…		…
565	* causing enormous grief in return for some better fake benchmark numbers.	650	* causing enormous grief in return for some better fake benchmark numbers.
566	* or so.	651	* or so.
567	* we try to detect these and simply assume they are not gcc - if they have	652	* 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.	653	* an issue with that they should have done it right in the first place.
569	*/	654	*/
570	#ifndef ECB_GCC_VERSION
571	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__	655	#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	656	#define ECB_GCC_VERSION(major,minor) 0
573	#else	657	#else
574	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))	658	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))
575	#endif	659	#endif
576	#endif
577		660
578	#define ECB_C (__STDC__+0) /* this assumes that __STDC__ is either empty or a number */	661	#define ECB_CLANG_VERSION(major,minor) (__clang_major__ > (major) || (__clang_major__ == (major) && __clang_minor__ >= (minor)))
579	#define ECB_C99 (__STDC_VERSION__ >= 199901L)	662
580	#define ECB_C11 (__STDC_VERSION__ >= 201112L)	663	#if __clang__ && defined __has_builtin
		664	#define ECB_CLANG_BUILTIN(x) __has_builtin (x)
		665	#else
		666	#define ECB_CLANG_BUILTIN(x) 0
		667	#endif
		668
		669	#if __clang__ && defined __has_extension
		670	#define ECB_CLANG_EXTENSION(x) __has_extension (x)
		671	#else
		672	#define ECB_CLANG_EXTENSION(x) 0
		673	#endif
		674
581	#define ECB_CPP (__cplusplus+0)	675	#define ECB_CPP (__cplusplus+0)
582	#define ECB_CPP11 (__cplusplus >= 201103L)	676	#define ECB_CPP11 (__cplusplus >= 201103L)
		677	#define ECB_CPP14 (__cplusplus >= 201402L)
		678	#define ECB_CPP17 (__cplusplus >= 201703L)
		679
		680	#if ECB_CPP
		681	#define ECB_C 0
		682	#define ECB_STDC_VERSION 0
		683	#else
		684	#define ECB_C 1
		685	#define ECB_STDC_VERSION __STDC_VERSION__
		686	#endif
		687
		688	#define ECB_C99 (ECB_STDC_VERSION >= 199901L)
		689	#define ECB_C11 (ECB_STDC_VERSION >= 201112L)
		690	#define ECB_C17 (ECB_STDC_VERSION >= 201710L)
583		691
584	#if ECB_CPP	692	#if ECB_CPP
585	#define ECB_EXTERN_C extern "C"	693	#define ECB_EXTERN_C extern "C"
586	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {	694	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {
587	#define ECB_EXTERN_C_END }	695	#define ECB_EXTERN_C_END }
…		…
602		710
603	#if ECB_NO_SMP	711	#if ECB_NO_SMP
604	#define ECB_MEMORY_FENCE do { } while (0)	712	#define ECB_MEMORY_FENCE do { } while (0)
605	#endif	713	#endif
606		714
		715	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/compiler_ref/compiler_builtins.html */
		716	#if __xlC__ && ECB_CPP
		717	#include <builtins.h>
		718	#endif
		719
		720	#if 1400 <= _MSC_VER
		721	#include <intrin.h> /* fence functions _ReadBarrier, also bit search functions _BitScanReverse */
		722	#endif
		723
607	#ifndef ECB_MEMORY_FENCE	724	#ifndef ECB_MEMORY_FENCE
608	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	725	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
		726	#define ECB_MEMORY_FENCE_RELAXED __asm__ __volatile__ ("" : : : "memory")
609	#if __i386 || __i386__	727	#if __i386 || __i386__
610	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")	728	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")
611	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")	729	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
612	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	730	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
613	#elif __amd64 || __amd64__ || __x86_64 || __x86_64__	731	#elif ECB_GCC_AMD64
614	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")	732	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")
615	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")	733	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
616	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	734	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
617	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__	735	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__
618	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")	736	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")
		737	#elif defined __ARM_ARCH_2__ \
		738	|| defined __ARM_ARCH_3__ || defined __ARM_ARCH_3M__ \
		739	|| defined __ARM_ARCH_4__ || defined __ARM_ARCH_4T__ \
		740	|| defined __ARM_ARCH_5__ || defined __ARM_ARCH_5E__ \
		741	|| defined __ARM_ARCH_5T__ || defined __ARM_ARCH_5TE__ \
		742	|| defined __ARM_ARCH_5TEJ__
		743	/* 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__ \	744	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \
620	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__	745	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__ \
		746	|| defined __ARM_ARCH_6T2__
621	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")	747	#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__ \	748	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \
623	|| defined __ARM_ARCH_7M__ || defined __ARM_ARCH_7R__	749	|| defined __ARM_ARCH_7R__ || defined __ARM_ARCH_7M__
624	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")	750	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")
625	#elif __sparc || __sparc__	751	#elif __aarch64__
		752	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb ish" : : : "memory")
		753	#elif (__sparc || __sparc__) && !(__sparc_v8__ || defined __sparcv8)
626	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")	754	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")
627	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")	755	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")
628	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")	756	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")
629	#elif defined __s390__ || defined __s390x__	757	#elif defined __s390__ || defined __s390x__
630	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")	758	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")
…		…
651		779
652	#ifndef ECB_MEMORY_FENCE	780	#ifndef ECB_MEMORY_FENCE
653	#if ECB_GCC_VERSION(4,7)	781	#if ECB_GCC_VERSION(4,7)
654	/* see comment below (stdatomic.h) about the C11 memory model. */	782	/* see comment below (stdatomic.h) about the C11 memory model. */
655	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)	783	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)
		784	#define ECB_MEMORY_FENCE_ACQUIRE __atomic_thread_fence (__ATOMIC_ACQUIRE)
		785	#define ECB_MEMORY_FENCE_RELEASE __atomic_thread_fence (__ATOMIC_RELEASE)
		786	#define ECB_MEMORY_FENCE_RELAXED __atomic_thread_fence (__ATOMIC_RELAXED)
656		787
657	/* The __has_feature syntax from clang is so misdesigned that we cannot use it	788	#elif ECB_CLANG_EXTENSION(c_atomic)
658	* without risking compile time errors with other compilers. We *could*
659	* define our own ecb_clang_has_feature, but I just can't be bothered to work
660	* around this shit time and again.
661	* #elif defined __clang && __has_feature (cxx_atomic)
662	* // see comment below (stdatomic.h) about the C11 memory model.	789	/* see comment below (stdatomic.h) about the C11 memory model. */
663	* #define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)	790	#define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)
664	*/	791	#define ECB_MEMORY_FENCE_ACQUIRE __c11_atomic_thread_fence (__ATOMIC_ACQUIRE)
		792	#define ECB_MEMORY_FENCE_RELEASE __c11_atomic_thread_fence (__ATOMIC_RELEASE)
		793	#define ECB_MEMORY_FENCE_RELAXED __c11_atomic_thread_fence (__ATOMIC_RELAXED)
665		794
666	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__	795	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__
667	#define ECB_MEMORY_FENCE __sync_synchronize ()	796	#define ECB_MEMORY_FENCE __sync_synchronize ()
		797	#elif _MSC_VER >= 1500 /* VC++ 2008 */
		798	/* apparently, microsoft broke all the memory barrier stuff in Visual Studio 2008... */
		799	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)
		800	#define ECB_MEMORY_FENCE _ReadWriteBarrier (); MemoryBarrier()
		801	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier (); MemoryBarrier() /* according to msdn, _ReadBarrier is not a load fence */
		802	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier (); MemoryBarrier()
668	#elif _MSC_VER >= 1400 /* VC++ 2005 */	803	#elif _MSC_VER >= 1400 /* VC++ 2005 */
669	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)	804	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)
670	#define ECB_MEMORY_FENCE _ReadWriteBarrier ()	805	#define ECB_MEMORY_FENCE _ReadWriteBarrier ()
671	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier () /* according to msdn, _ReadBarrier is not a load fence */	806	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier () /* according to msdn, _ReadBarrier is not a load fence */
672	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier ()	807	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier ()
673	#elif defined _WIN32	808	#elif defined _WIN32
674	#include <WinNT.h>	809	#include <WinNT.h>
675	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */	810	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */
676	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	811	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
677	#include <mbarrier.h>	812	#include <mbarrier.h>
678	#define ECB_MEMORY_FENCE __machine_rw_barrier ()	813	#define ECB_MEMORY_FENCE __machine_rw_barrier ()
679	#define ECB_MEMORY_FENCE_ACQUIRE __machine_r_barrier ()	814	#define ECB_MEMORY_FENCE_ACQUIRE __machine_acq_barrier ()
680	#define ECB_MEMORY_FENCE_RELEASE __machine_w_barrier ()	815	#define ECB_MEMORY_FENCE_RELEASE __machine_rel_barrier ()
		816	#define ECB_MEMORY_FENCE_RELAXED __compiler_barrier ()
681	#elif __xlC__	817	#elif __xlC__
682	#define ECB_MEMORY_FENCE __sync ()	818	#define ECB_MEMORY_FENCE __sync ()
683	#endif	819	#endif
684	#endif	820	#endif
685		821
686	#ifndef ECB_MEMORY_FENCE	822	#ifndef ECB_MEMORY_FENCE
687	#if ECB_C11 && !defined __STDC_NO_ATOMICS__	823	#if ECB_C11 && !defined __STDC_NO_ATOMICS__
688	/* we assume that these memory fences work on all variables/all memory accesses, */	824	/* we assume that these memory fences work on all variables/all memory accesses, */
689	/* not just C11 atomics and atomic accesses */	825	/* not just C11 atomics and atomic accesses */
690	#include <stdatomic.h>	826	#include <stdatomic.h>
691	/* Unfortunately, neither gcc 4.7 nor clang 3.1 generate any instructions for */
692	/* any fence other than seq_cst, which isn't very efficient for us. */
693	/* Why that is, we don't know - either the C11 memory model is quite useless */
694	/* for most usages, or gcc and clang have a bug */
695	/* I *currently* lean towards the latter, and inefficiently implement */
696	/* all three of ecb's fences as a seq_cst fence */
697	#define ECB_MEMORY_FENCE atomic_thread_fence (memory_order_seq_cst)	827	#define ECB_MEMORY_FENCE atomic_thread_fence (memory_order_seq_cst)
		828	#define ECB_MEMORY_FENCE_ACQUIRE atomic_thread_fence (memory_order_acquire)
		829	#define ECB_MEMORY_FENCE_RELEASE atomic_thread_fence (memory_order_release)
698	#endif	830	#endif
699	#endif	831	#endif
700		832
701	#ifndef ECB_MEMORY_FENCE	833	#ifndef ECB_MEMORY_FENCE
702	#if !ECB_AVOID_PTHREADS	834	#if !ECB_AVOID_PTHREADS
…		…
722		854
723	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE	855	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE
724	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	856	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
725	#endif	857	#endif
726		858
		859	#if !defined ECB_MEMORY_FENCE_RELAXED && defined ECB_MEMORY_FENCE
		860	#define ECB_MEMORY_FENCE_RELAXED ECB_MEMORY_FENCE /* very heavy-handed */
		861	#endif
		862
727	/*****************************************************************************/	863	/*****************************************************************************/
728		864
729	#if __cplusplus	865	#if ECB_CPP
730	#define ecb_inline static inline	866	#define ecb_inline static inline
731	#elif ECB_GCC_VERSION(2,5)	867	#elif ECB_GCC_VERSION(2,5)
732	#define ecb_inline static __inline__	868	#define ecb_inline static __inline__
733	#elif ECB_C99	869	#elif ECB_C99
734	#define ecb_inline static inline	870	#define ecb_inline static inline
…		…
748		884
749	#define ECB_CONCAT_(a, b) a ## b	885	#define ECB_CONCAT_(a, b) a ## b
750	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)	886	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)
751	#define ECB_STRINGIFY_(a) # a	887	#define ECB_STRINGIFY_(a) # a
752	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)	888	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)
		889	#define ECB_STRINGIFY_EXPR(expr) ((expr), ECB_STRINGIFY_ (expr))
753		890
754	#define ecb_function_ ecb_inline	891	#define ecb_function_ ecb_inline
755		892
756	#if ECB_GCC_VERSION(3,1)	893	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_VERSION(2,8)
757	#define ecb_attribute(attrlist) __attribute__(attrlist)	894	#define ecb_attribute(attrlist) __attribute__ (attrlist)
		895	#else
		896	#define ecb_attribute(attrlist)
		897	#endif
		898
		899	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_constant_p)
758	#define ecb_is_constant(expr) __builtin_constant_p (expr)	900	#define ecb_is_constant(expr) __builtin_constant_p (expr)
		901	#else
		902	/* possible C11 impl for integral types
		903	typedef struct ecb_is_constant_struct ecb_is_constant_struct;
		904	#define ecb_is_constant(expr) _Generic ((1 ? (struct ecb_is_constant_struct *)0 : (void *)((expr) - (expr)), ecb_is_constant_struct *: 0, default: 1)) */
		905
		906	#define ecb_is_constant(expr) 0
		907	#endif
		908
		909	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_expect)
759	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))	910	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))
		911	#else
		912	#define ecb_expect(expr,value) (expr)
		913	#endif
		914
		915	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_prefetch)
760	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)	916	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)
761	#else	917	#else
762	#define ecb_attribute(attrlist)
763	#define ecb_is_constant(expr) 0
764	#define ecb_expect(expr,value) (expr)
765	#define ecb_prefetch(addr,rw,locality)	918	#define ecb_prefetch(addr,rw,locality)
766	#endif	919	#endif
767		920
768	/* no emulation for ecb_decltype */	921	/* no emulation for ecb_decltype */
769	#if ECB_GCC_VERSION(4,5)	922	#if ECB_CPP11
		923	// older implementations might have problems with decltype(x)::type, work around it
		924	template<class T> struct ecb_decltype_t { typedef T type; };
770	#define ecb_decltype(x) __decltype(x)	925	#define ecb_decltype(x) ecb_decltype_t<decltype (x)>::type
771	#elif ECB_GCC_VERSION(3,0)	926	#elif ECB_GCC_VERSION(3,0) || ECB_CLANG_VERSION(2,8)
772	#define ecb_decltype(x) __typeof(x)	927	#define ecb_decltype(x) __typeof__ (x)
773	#endif	928	#endif
774		929
		930	#if _MSC_VER >= 1300
		931	#define ecb_deprecated __declspec (deprecated)
		932	#else
		933	#define ecb_deprecated ecb_attribute ((__deprecated__))
		934	#endif
		935
		936	#if _MSC_VER >= 1500
		937	#define ecb_deprecated_message(msg) __declspec (deprecated (msg))
		938	#elif ECB_GCC_VERSION(4,5)
		939	#define ecb_deprecated_message(msg) ecb_attribute ((__deprecated__ (msg))
		940	#else
		941	#define ecb_deprecated_message(msg) ecb_deprecated
		942	#endif
		943
		944	#if _MSC_VER >= 1400
		945	#define ecb_noinline __declspec (noinline)
		946	#else
775	#define ecb_noinline ecb_attribute ((__noinline__))	947	#define ecb_noinline ecb_attribute ((__noinline__))
		948	#endif
		949
776	#define ecb_unused ecb_attribute ((__unused__))	950	#define ecb_unused ecb_attribute ((__unused__))
777	#define ecb_const ecb_attribute ((__const__))	951	#define ecb_const ecb_attribute ((__const__))
778	#define ecb_pure ecb_attribute ((__pure__))	952	#define ecb_pure ecb_attribute ((__pure__))
779		953
780	#if ECB_C11	954	#if ECB_C11 || __IBMC_NORETURN
		955	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/language_ref/noreturn.html */
781	#define ecb_noreturn _Noreturn	956	#define ecb_noreturn _Noreturn
		957	#elif ECB_CPP11
		958	#define ecb_noreturn [[noreturn]]
		959	#elif _MSC_VER >= 1200
		960	/* http://msdn.microsoft.com/en-us/library/k6ktzx3s.aspx */
		961	#define ecb_noreturn __declspec (noreturn)
782	#else	962	#else
783	#define ecb_noreturn ecb_attribute ((__noreturn__))	963	#define ecb_noreturn ecb_attribute ((__noreturn__))
784	#endif	964	#endif
785		965
786	#if ECB_GCC_VERSION(4,3)	966	#if ECB_GCC_VERSION(4,3)
…		…
801	/* for compatibility to the rest of the world */	981	/* for compatibility to the rest of the world */
802	#define ecb_likely(expr) ecb_expect_true (expr)	982	#define ecb_likely(expr) ecb_expect_true (expr)
803	#define ecb_unlikely(expr) ecb_expect_false (expr)	983	#define ecb_unlikely(expr) ecb_expect_false (expr)
804		984
805	/* count trailing zero bits and count # of one bits */	985	/* count trailing zero bits and count # of one bits */
806	#if ECB_GCC_VERSION(3,4)	986	#if ECB_GCC_VERSION(3,4) \
		987	|| (ECB_CLANG_BUILTIN(__builtin_clz) && ECB_CLANG_BUILTIN(__builtin_clzll) \
		988	&& ECB_CLANG_BUILTIN(__builtin_ctz) && ECB_CLANG_BUILTIN(__builtin_ctzll) \
		989	&& ECB_CLANG_BUILTIN(__builtin_popcount))
807	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */	990	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */
808	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)	991	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)
809	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)	992	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)
810	#define ecb_ctz32(x) __builtin_ctz (x)	993	#define ecb_ctz32(x) __builtin_ctz (x)
811	#define ecb_ctz64(x) __builtin_ctzll (x)	994	#define ecb_ctz64(x) __builtin_ctzll (x)
812	#define ecb_popcount32(x) __builtin_popcount (x)	995	#define ecb_popcount32(x) __builtin_popcount (x)
813	/* no popcountll */	996	/* no popcountll */
814	#else	997	#else
815	ecb_function_ int ecb_ctz32 (uint32_t x) ecb_const;	998	ecb_function_ ecb_const int ecb_ctz32 (uint32_t x);
816	ecb_function_ int	999	ecb_function_ ecb_const int
817	ecb_ctz32 (uint32_t x)	1000	ecb_ctz32 (uint32_t x)
818	{	1001	{
		1002	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		1003	unsigned long r;
		1004	_BitScanForward (&r, x);
		1005	return (int)r;
		1006	#else
819	int r = 0;	1007	int r = 0;
820		1008
821	x &= ~x + 1; /* this isolates the lowest bit */	1009	x &= ~x + 1; /* this isolates the lowest bit */
822		1010
823	#if ECB_branchless_on_i386	1011	#if ECB_branchless_on_i386
…		…
833	if (x & 0xff00ff00) r += 8;	1021	if (x & 0xff00ff00) r += 8;
834	if (x & 0xffff0000) r += 16;	1022	if (x & 0xffff0000) r += 16;
835	#endif	1023	#endif
836		1024
837	return r;	1025	return r;
		1026	#endif
838	}	1027	}
839		1028
840	ecb_function_ int ecb_ctz64 (uint64_t x) ecb_const;	1029	ecb_function_ ecb_const int ecb_ctz64 (uint64_t x);
841	ecb_function_ int	1030	ecb_function_ ecb_const int
842	ecb_ctz64 (uint64_t x)	1031	ecb_ctz64 (uint64_t x)
843	{	1032	{
		1033	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1034	unsigned long r;
		1035	_BitScanForward64 (&r, x);
		1036	return (int)r;
		1037	#else
844	int shift = x & 0xffffffffU ? 0 : 32;	1038	int shift = x & 0xffffffff ? 0 : 32;
845	return ecb_ctz32 (x >> shift) + shift;	1039	return ecb_ctz32 (x >> shift) + shift;
		1040	#endif
846	}	1041	}
847		1042
848	ecb_function_ int ecb_popcount32 (uint32_t x) ecb_const;	1043	ecb_function_ ecb_const int ecb_popcount32 (uint32_t x);
849	ecb_function_ int	1044	ecb_function_ ecb_const int
850	ecb_popcount32 (uint32_t x)	1045	ecb_popcount32 (uint32_t x)
851	{	1046	{
852	x -= (x >> 1) & 0x55555555;	1047	x -= (x >> 1) & 0x55555555;
853	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);	1048	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);
854	x = ((x >> 4) + x) & 0x0f0f0f0f;	1049	x = ((x >> 4) + x) & 0x0f0f0f0f;
855	x *= 0x01010101;	1050	x *= 0x01010101;
856		1051
857	return x >> 24;	1052	return x >> 24;
858	}	1053	}
859		1054
860	ecb_function_ int ecb_ld32 (uint32_t x) ecb_const;	1055	ecb_function_ ecb_const int ecb_ld32 (uint32_t x);
861	ecb_function_ int ecb_ld32 (uint32_t x)	1056	ecb_function_ ecb_const int ecb_ld32 (uint32_t x)
862	{	1057	{
		1058	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		1059	unsigned long r;
		1060	_BitScanReverse (&r, x);
		1061	return (int)r;
		1062	#else
863	int r = 0;	1063	int r = 0;
864		1064
865	if (x >> 16) { x >>= 16; r += 16; }	1065	if (x >> 16) { x >>= 16; r += 16; }
866	if (x >> 8) { x >>= 8; r += 8; }	1066	if (x >> 8) { x >>= 8; r += 8; }
867	if (x >> 4) { x >>= 4; r += 4; }	1067	if (x >> 4) { x >>= 4; r += 4; }
868	if (x >> 2) { x >>= 2; r += 2; }	1068	if (x >> 2) { x >>= 2; r += 2; }
869	if (x >> 1) { r += 1; }	1069	if (x >> 1) { r += 1; }
870		1070
871	return r;	1071	return r;
		1072	#endif
872	}	1073	}
873		1074
874	ecb_function_ int ecb_ld64 (uint64_t x) ecb_const;	1075	ecb_function_ ecb_const int ecb_ld64 (uint64_t x);
875	ecb_function_ int ecb_ld64 (uint64_t x)	1076	ecb_function_ ecb_const int ecb_ld64 (uint64_t x)
876	{	1077	{
		1078	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1079	unsigned long r;
		1080	_BitScanReverse64 (&r, x);
		1081	return (int)r;
		1082	#else
877	int r = 0;	1083	int r = 0;
878		1084
879	if (x >> 32) { x >>= 32; r += 32; }	1085	if (x >> 32) { x >>= 32; r += 32; }
880		1086
881	return r + ecb_ld32 (x);	1087	return r + ecb_ld32 (x);
		1088	#endif
882	}	1089	}
883	#endif	1090	#endif
884		1091
885	ecb_function_ ecb_bool ecb_is_pot32 (uint32_t x) ecb_const;	1092	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x);
886	ecb_function_ ecb_bool ecb_is_pot32 (uint32_t x) { return !(x & (x - 1)); }	1093	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x) { return !(x & (x - 1)); }
887	ecb_function_ ecb_bool ecb_is_pot64 (uint64_t x) ecb_const;	1094	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x);
888	ecb_function_ ecb_bool ecb_is_pot64 (uint64_t x) { return !(x & (x - 1)); }	1095	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x) { return !(x & (x - 1)); }
889		1096
890	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x) ecb_const;	1097	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x);
891	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x)	1098	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x)
892	{	1099	{
893	return ( (x * 0x0802U & 0x22110U)	1100	return ( (x * 0x0802U & 0x22110U)
894	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;	1101	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;
895	}	1102	}
896		1103
897	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x) ecb_const;	1104	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x);
898	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x)	1105	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x)
899	{	1106	{
900	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);	1107	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);
901	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);	1108	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);
902	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);	1109	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);
903	x = ( x >> 8 ) | ( x << 8);	1110	x = ( x >> 8 ) | ( x << 8);
904		1111
905	return x;	1112	return x;
906	}	1113	}
907		1114
908	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x) ecb_const;	1115	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x);
909	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x)	1116	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x)
910	{	1117	{
911	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);	1118	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);
912	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);	1119	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);
913	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);	1120	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);
914	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);	1121	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);
…		…
917	return x;	1124	return x;
918	}	1125	}
919		1126
920	/* popcount64 is only available on 64 bit cpus as gcc builtin */	1127	/* popcount64 is only available on 64 bit cpus as gcc builtin */
921	/* so for this version we are lazy */	1128	/* so for this version we are lazy */
922	ecb_function_ int ecb_popcount64 (uint64_t x) ecb_const;	1129	ecb_function_ ecb_const int ecb_popcount64 (uint64_t x);
923	ecb_function_ int	1130	ecb_function_ ecb_const int
924	ecb_popcount64 (uint64_t x)	1131	ecb_popcount64 (uint64_t x)
925	{	1132	{
926	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);	1133	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);
927	}	1134	}
928		1135
929	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) ecb_const;	1136	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count);
930	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) ecb_const;	1137	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count);
931	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) ecb_const;	1138	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count);
932	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) ecb_const;	1139	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count);
933	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) ecb_const;	1140	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count);
934	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) ecb_const;	1141	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count);
935	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) ecb_const;	1142	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count);
936	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) ecb_const;	1143	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count);
937		1144
938	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }	1145	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }
939	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }	1146	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }
940	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }	1147	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }
941	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }	1148	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }
942	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }	1149	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }
943	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }	1150	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }
944	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }	1151	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }
945	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }	1152	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }
946		1153
947	#if ECB_GCC_VERSION(4,3)	1154	#if ECB_GCC_VERSION(4,3) || (ECB_CLANG_BUILTIN(__builtin_bswap32) && ECB_CLANG_BUILTIN(__builtin_bswap64))
		1155	#if ECB_GCC_VERSION(4,8) || ECB_CLANG_BUILTIN(__builtin_bswap16)
		1156	#define ecb_bswap16(x) __builtin_bswap16 (x)
		1157	#else
948	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)	1158	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)
		1159	#endif
949	#define ecb_bswap32(x) __builtin_bswap32 (x)	1160	#define ecb_bswap32(x) __builtin_bswap32 (x)
950	#define ecb_bswap64(x) __builtin_bswap64 (x)	1161	#define ecb_bswap64(x) __builtin_bswap64 (x)
		1162	#elif _MSC_VER
		1163	#include <stdlib.h>
		1164	#define ecb_bswap16(x) ((uint16_t)_byteswap_ushort ((uint16_t)(x)))
		1165	#define ecb_bswap32(x) ((uint32_t)_byteswap_ulong ((uint32_t)(x)))
		1166	#define ecb_bswap64(x) ((uint64_t)_byteswap_uint64 ((uint64_t)(x)))
951	#else	1167	#else
952	ecb_function_ uint16_t ecb_bswap16 (uint16_t x) ecb_const;	1168	ecb_function_ ecb_const uint16_t ecb_bswap16 (uint16_t x);
953	ecb_function_ uint16_t	1169	ecb_function_ ecb_const uint16_t
954	ecb_bswap16 (uint16_t x)	1170	ecb_bswap16 (uint16_t x)
955	{	1171	{
956	return ecb_rotl16 (x, 8);	1172	return ecb_rotl16 (x, 8);
957	}	1173	}
958		1174
959	ecb_function_ uint32_t ecb_bswap32 (uint32_t x) ecb_const;	1175	ecb_function_ ecb_const uint32_t ecb_bswap32 (uint32_t x);
960	ecb_function_ uint32_t	1176	ecb_function_ ecb_const uint32_t
961	ecb_bswap32 (uint32_t x)	1177	ecb_bswap32 (uint32_t x)
962	{	1178	{
963	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);	1179	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);
964	}	1180	}
965		1181
966	ecb_function_ uint64_t ecb_bswap64 (uint64_t x) ecb_const;	1182	ecb_function_ ecb_const uint64_t ecb_bswap64 (uint64_t x);
967	ecb_function_ uint64_t	1183	ecb_function_ ecb_const uint64_t
968	ecb_bswap64 (uint64_t x)	1184	ecb_bswap64 (uint64_t x)
969	{	1185	{
970	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);	1186	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);
971	}	1187	}
972	#endif	1188	#endif
973		1189
974	#if ECB_GCC_VERSION(4,5)	1190	#if ECB_GCC_VERSION(4,5) || ECB_CLANG_BUILTIN(__builtin_unreachable)
975	#define ecb_unreachable() __builtin_unreachable ()	1191	#define ecb_unreachable() __builtin_unreachable ()
976	#else	1192	#else
977	/* this seems to work fine, but gcc always emits a warning for it :/ */	1193	/* this seems to work fine, but gcc always emits a warning for it :/ */
978	ecb_inline void ecb_unreachable (void) ecb_noreturn;	1194	ecb_inline ecb_noreturn void ecb_unreachable (void);
979	ecb_inline void ecb_unreachable (void) { }	1195	ecb_inline ecb_noreturn void ecb_unreachable (void) { }
980	#endif	1196	#endif
981		1197
982	/* try to tell the compiler that some condition is definitely true */	1198	/* try to tell the compiler that some condition is definitely true */
983	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0	1199	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0
984		1200
985	ecb_inline unsigned char ecb_byteorder_helper (void) ecb_const;	1201	ecb_inline ecb_const uint32_t ecb_byteorder_helper (void);
986	ecb_inline unsigned char	1202	ecb_inline ecb_const uint32_t
987	ecb_byteorder_helper (void)	1203	ecb_byteorder_helper (void)
988	{	1204	{
989	/* the union code still generates code under pressure in gcc, */	1205	/* the union code still generates code under pressure in gcc, */
990	/* but less than using pointers, and always seems to */	1206	/* but less than using pointers, and always seems to */
991	/* successfully return a constant. */	1207	/* successfully return a constant. */
992	/* the reason why we have this horrible preprocessor mess */	1208	/* the reason why we have this horrible preprocessor mess */
993	/* is to avoid it in all cases, at least on common architectures */	1209	/* is to avoid it in all cases, at least on common architectures */
994	/* or when using a recent enough gcc version (>= 4.6) */	1210	/* or when using a recent enough gcc version (>= 4.6) */
995	#if __i386 || __i386__ || _M_X86 || __amd64 || __amd64__ || _M_X64
996	return 0x44;
997	#elif __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_LITTLE_ENDIAN__	1211	#if (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_LITTLE_ENDIAN__) \
		1212	|| ((__i386 || __i386__ || _M_IX86 || ECB_GCC_AMD64 || ECB_MSVC_AMD64) && !__VOS__)
		1213	#define ECB_LITTLE_ENDIAN 1
998	return 0x44;	1214	return 0x44332211;
999	#elif __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__	1215	#elif (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__) \
		1216	|| ((__AARCH64EB__ || __MIPSEB__ || __ARMEB__) && !__VOS__)
		1217	#define ECB_BIG_ENDIAN 1
1000	return 0x11;	1218	return 0x11223344;
1001	#else	1219	#else
1002	union	1220	union
1003	{	1221	{
		1222	uint8_t c[4];
1004	uint32_t i;	1223	uint32_t u;
1005	uint8_t c;
1006	} u = { 0x11223344 };	1224	} u = { 0x11, 0x22, 0x33, 0x44 };
1007	return u.c;	1225	return u.u;
1008	#endif	1226	#endif
1009	}	1227	}
1010		1228
1011	ecb_inline ecb_bool ecb_big_endian (void) ecb_const;	1229	ecb_inline ecb_const ecb_bool ecb_big_endian (void);
1012	ecb_inline ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11; }	1230	ecb_inline ecb_const ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11223344; }
1013	ecb_inline ecb_bool ecb_little_endian (void) ecb_const;	1231	ecb_inline ecb_const ecb_bool ecb_little_endian (void);
1014	ecb_inline ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44; }	1232	ecb_inline ecb_const ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44332211; }
1015		1233
1016	#if ECB_GCC_VERSION(3,0) || ECB_C99	1234	#if ECB_GCC_VERSION(3,0) || ECB_C99
1017	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))	1235	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))
1018	#else	1236	#else
1019	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))	1237	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))
1020	#endif	1238	#endif
1021		1239
1022	#if __cplusplus	1240	#if ECB_CPP
1023	template<typename T>	1241	template<typename T>
1024	static inline T ecb_div_rd (T val, T div)	1242	static inline T ecb_div_rd (T val, T div)
1025	{	1243	{
1026	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;	1244	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;
1027	}	1245	}
…		…
1044	}	1262	}
1045	#else	1263	#else
1046	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))	1264	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))
1047	#endif	1265	#endif
1048		1266
		1267	ecb_function_ ecb_const uint32_t ecb_binary16_to_binary32 (uint32_t x);
		1268	ecb_function_ ecb_const uint32_t
		1269	ecb_binary16_to_binary32 (uint32_t x)
		1270	{
		1271	unsigned int s = (x & 0x8000) << (31 - 15);
		1272	int e = (x >> 10) & 0x001f;
		1273	unsigned int m = x & 0x03ff;
		1274
		1275	if (ecb_expect_false (e == 31))
		1276	/* infinity or NaN */
		1277	e = 255 - (127 - 15);
		1278	else if (ecb_expect_false (!e))
		1279	{
		1280	if (ecb_expect_true (!m))
		1281	/* zero, handled by code below by forcing e to 0 */
		1282	e = 0 - (127 - 15);
		1283	else
		1284	{
		1285	/* subnormal, renormalise */
		1286	unsigned int s = 10 - ecb_ld32 (m);
		1287
		1288	m = (m << s) & 0x3ff; /* mask implicit bit */
		1289	e -= s - 1;
		1290	}
		1291	}
		1292
		1293	/* e and m now are normalised, or zero, (or inf or nan) */
		1294	e += 127 - 15;
		1295
		1296	return s | (e << 23) | (m << (23 - 10));
		1297	}
		1298
		1299	ecb_function_ ecb_const uint16_t ecb_binary32_to_binary16 (uint32_t x);
		1300	ecb_function_ ecb_const uint16_t
		1301	ecb_binary32_to_binary16 (uint32_t x)
		1302	{
		1303	unsigned int s = (x >> 16) & 0x00008000; /* sign bit, the easy part */
		1304	unsigned int e = ((x >> 23) & 0x000000ff) - (127 - 15); /* the desired exponent */
		1305	unsigned int m = x & 0x007fffff;
		1306
		1307	x &= 0x7fffffff;
		1308
		1309	/* if it's within range of binary16 normals, use fast path */
		1310	if (ecb_expect_true (0x38800000 <= x && x <= 0x477fefff))
		1311	{
		1312	/* mantissa round-to-even */
		1313	m += 0x00000fff + ((m >> (23 - 10)) & 1);
		1314
		1315	/* handle overflow */
		1316	if (ecb_expect_false (m >= 0x00800000))
		1317	{
		1318	m >>= 1;
		1319	e += 1;
		1320	}
		1321
		1322	return s | (e << 10) | (m >> (23 - 10));
		1323	}
		1324
		1325	/* handle large numbers and infinity */
		1326	if (ecb_expect_true (0x477fefff < x && x <= 0x7f800000))
		1327	return s | 0x7c00;
		1328
		1329	/* handle zero, subnormals and small numbers */
		1330	if (ecb_expect_true (x < 0x38800000))
		1331	{
		1332	/* zero */
		1333	if (ecb_expect_true (!x))
		1334	return s;
		1335
		1336	/* handle subnormals */
		1337
		1338	/* too small, will be zero */
		1339	if (e < (14 - 24)) /* might not be sharp, but is good enough */
		1340	return s;
		1341
		1342	m |= 0x00800000; /* make implicit bit explicit */
		1343
		1344	/* very tricky - we need to round to the nearest e (+10) bit value */
		1345	{
		1346	unsigned int bits = 14 - e;
		1347	unsigned int half = (1 << (bits - 1)) - 1;
		1348	unsigned int even = (m >> bits) & 1;
		1349
		1350	/* if this overflows, we will end up with a normalised number */
		1351	m = (m + half + even) >> bits;
		1352	}
		1353
		1354	return s | m;
		1355	}
		1356
		1357	/* handle NaNs, preserve leftmost nan bits, but make sure we don't turn them into infinities */
		1358	m >>= 13;
		1359
		1360	return s | 0x7c00 | m | !m;
		1361	}
		1362
1049	/*******************************************************************************/	1363	/*******************************************************************************/
1050	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */	1364	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */
1051		1365
1052	/* basically, everything uses "ieee pure-endian" floating point numbers */	1366	/* basically, everything uses "ieee pure-endian" floating point numbers */
1053	/* the only noteworthy exception is ancient armle, which uses order 43218765 */	1367	/* the only noteworthy exception is ancient armle, which uses order 43218765 */
1054	#if 0 \	1368	#if 0 \
1055	|| __i386 || __i386__ \	1369	|| __i386 || __i386__ \
1056	|| __amd64 || __amd64__ || __x86_64 || __x86_64__ \	1370	|| ECB_GCC_AMD64 \
1057	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \	1371	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \
1058	|| defined __arm__ && defined __ARM_EABI__ \
1059	|| defined __s390__ || defined __s390x__ \	1372	|| defined __s390__ || defined __s390x__ \
1060	|| defined __mips__ \	1373	|| defined __mips__ \
1061	|| defined __alpha__ \	1374	|| defined __alpha__ \
1062	|| defined __hppa__ \	1375	|| defined __hppa__ \
1063	|| defined __ia64__ \	1376	|| defined __ia64__ \
1064	|| defined __m68k__ \	1377	|| defined __m68k__ \
1065	|| defined __m88k__ \	1378	|| defined __m88k__ \
1066	|| defined __sh__ \	1379	|| defined __sh__ \
1067	|| defined _M_IX86 || defined _M_AMD64 || defined _M_IA64	1380	|| defined _M_IX86 || defined ECB_MSVC_AMD64 || defined _M_IA64 \
		1381	|| (defined __arm__ && (defined __ARM_EABI__ || defined __EABI__ || defined __VFP_FP__ || defined _WIN32_WCE || defined __ANDROID__)) \
		1382	|| defined __aarch64__
1068	#define ECB_STDFP 1	1383	#define ECB_STDFP 1
1069	#include <string.h> /* for memcpy */	1384	#include <string.h> /* for memcpy */
1070	#else	1385	#else
1071	#define ECB_STDFP 0	1386	#define ECB_STDFP 0
1072	#endif	1387	#endif
1073		1388
1074	#ifndef ECB_NO_LIBM	1389	#ifndef ECB_NO_LIBM
1075		1390
1076	#include <math.h> /* for frexp*, ldexp*, INFINITY, NAN */	1391	#include <math.h> /* for frexp*, ldexp*, INFINITY, NAN */
1077		1392
		1393	/* only the oldest of old doesn't have this one. solaris. */
		1394	#ifdef INFINITY
		1395	#define ECB_INFINITY INFINITY
		1396	#else
		1397	#define ECB_INFINITY HUGE_VAL
		1398	#endif
		1399
1078	#ifdef NEN	1400	#ifdef NAN
1079	#define ECB_NAN NAN	1401	#define ECB_NAN NAN
1080	#else	1402	#else
1081	#define ECB_NAN INFINITY	1403	#define ECB_NAN ECB_INFINITY
1082	#endif	1404	#endif
1083		1405
1084	/* converts an ieee half/binary16 to a float */	1406	#if ECB_C99 || _XOPEN_VERSION >= 600 || _POSIX_VERSION >= 200112L
1085	ecb_function_ float ecb_binary16_to_float (uint16_t x) ecb_const;	1407	#define ecb_ldexpf(x,e) ldexpf ((x), (e))
1086	ecb_function_ float	1408	#define ecb_frexpf(x,e) frexpf ((x), (e))
1087	ecb_binary16_to_float (uint16_t x)	1409	#else
1088	{	1410	#define ecb_ldexpf(x,e) (float) ldexp ((double) (x), (e))
1089	int e = (x >> 10) & 0x1f;	1411	#define ecb_frexpf(x,e) (float) frexp ((double) (x), (e))
1090	int m = x & 0x3ff;	1412	#endif
1091	float r;
1092
1093	if (!e ) r = ldexpf (m , -24);
1094	else if (e != 31) r = ldexpf (m + 0x400, e - 25);
1095	else if (m ) r = ECB_NAN;
1096	else r = INFINITY;
1097
1098	return x & 0x8000 ? -r : r;
1099	}
1100		1413
1101	/* convert a float to ieee single/binary32 */	1414	/* convert a float to ieee single/binary32 */
1102	ecb_function_ uint32_t ecb_float_to_binary32 (float x) ecb_const;	1415	ecb_function_ ecb_const uint32_t ecb_float_to_binary32 (float x);
1103	ecb_function_ uint32_t	1416	ecb_function_ ecb_const uint32_t
1104	ecb_float_to_binary32 (float x)	1417	ecb_float_to_binary32 (float x)
1105	{	1418	{
1106	uint32_t r;	1419	uint32_t r;
1107		1420
1108	#if ECB_STDFP	1421	#if ECB_STDFP
…		…
1115	if (x == 0e0f ) return 0x00000000U;	1428	if (x == 0e0f ) return 0x00000000U;
1116	if (x > +3.40282346638528860e+38f) return 0x7f800000U;	1429	if (x > +3.40282346638528860e+38f) return 0x7f800000U;
1117	if (x < -3.40282346638528860e+38f) return 0xff800000U;	1430	if (x < -3.40282346638528860e+38f) return 0xff800000U;
1118	if (x != x ) return 0x7fbfffffU;	1431	if (x != x ) return 0x7fbfffffU;
1119		1432
1120	m = frexpf (x, &e) * 0x1000000U;	1433	m = ecb_frexpf (x, &e) * 0x1000000U;
1121		1434
1122	r = m & 0x80000000U;	1435	r = m & 0x80000000U;
1123		1436
1124	if (r)	1437	if (r)
1125	m = -m;	1438	m = -m;
…		…
1137		1450
1138	return r;	1451	return r;
1139	}	1452	}
1140		1453
1141	/* converts an ieee single/binary32 to a float */	1454	/* converts an ieee single/binary32 to a float */
1142	ecb_function_ float ecb_binary32_to_float (uint32_t x) ecb_const;	1455	ecb_function_ ecb_const float ecb_binary32_to_float (uint32_t x);
1143	ecb_function_ float	1456	ecb_function_ ecb_const float
1144	ecb_binary32_to_float (uint32_t x)	1457	ecb_binary32_to_float (uint32_t x)
1145	{	1458	{
1146	float r;	1459	float r;
1147		1460
1148	#if ECB_STDFP	1461	#if ECB_STDFP
…		…
1158	x |= 0x800000U;	1471	x |= 0x800000U;
1159	else	1472	else
1160	e = 1;	1473	e = 1;
1161		1474
1162	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */	1475	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */
1163	r = ldexpf (x * (0.5f / 0x800000U), e - 126);	1476	r = ecb_ldexpf (x * (0.5f / 0x800000U), e - 126);
1164		1477
1165	r = neg ? -r : r;	1478	r = neg ? -r : r;
1166	#endif	1479	#endif
1167		1480
1168	return r;	1481	return r;
1169	}	1482	}
1170		1483
1171	/* convert a double to ieee double/binary64 */	1484	/* convert a double to ieee double/binary64 */
1172	ecb_function_ uint64_t ecb_double_to_binary64 (double x) ecb_const;	1485	ecb_function_ ecb_const uint64_t ecb_double_to_binary64 (double x);
1173	ecb_function_ uint64_t	1486	ecb_function_ ecb_const uint64_t
1174	ecb_double_to_binary64 (double x)	1487	ecb_double_to_binary64 (double x)
1175	{	1488	{
1176	uint64_t r;	1489	uint64_t r;
1177		1490
1178	#if ECB_STDFP	1491	#if ECB_STDFP
…		…
1207		1520
1208	return r;	1521	return r;
1209	}	1522	}
1210		1523
1211	/* converts an ieee double/binary64 to a double */	1524	/* converts an ieee double/binary64 to a double */
1212	ecb_function_ double ecb_binary64_to_double (uint64_t x) ecb_const;	1525	ecb_function_ ecb_const double ecb_binary64_to_double (uint64_t x);
1213	ecb_function_ double	1526	ecb_function_ ecb_const double
1214	ecb_binary64_to_double (uint64_t x)	1527	ecb_binary64_to_double (uint64_t x)
1215	{	1528	{
1216	double r;	1529	double r;
1217		1530
1218	#if ECB_STDFP	1531	#if ECB_STDFP
…		…
1236	#endif	1549	#endif
1237		1550
1238	return r;	1551	return r;
1239	}	1552	}
1240		1553
		1554	/* convert a float to ieee half/binary16 */
		1555	ecb_function_ ecb_const uint16_t ecb_float_to_binary16 (float x);
		1556	ecb_function_ ecb_const uint16_t
		1557	ecb_float_to_binary16 (float x)
		1558	{
		1559	return ecb_binary32_to_binary16 (ecb_float_to_binary32 (x));
		1560	}
		1561
		1562	/* convert an ieee half/binary16 to float */
		1563	ecb_function_ ecb_const float ecb_binary16_to_float (uint16_t x);
		1564	ecb_function_ ecb_const float
		1565	ecb_binary16_to_float (uint16_t x)
		1566	{
		1567	return ecb_binary32_to_float (ecb_binary16_to_binary32 (x));
		1568	}
		1569
1241	#endif	1570	#endif
1242		1571
1243	#endif	1572	#endif
1244		1573
1245	/* ECB.H END */	1574	/* ECB.H END */
1246		1575
1247	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS	1576	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS
1248	/* if your architecture doesn't need memory fences, e.g. because it is	1577	/* if your architecture doesn't need memory fences, e.g. because it is
1249	* single-cpu/core, or if you use libev in a project that doesn't use libev	1578	* single-cpu/core, or if you use libev in a project that doesn't use libev
1250	* from multiple threads, then you can define ECB_AVOID_PTHREADS when compiling	1579	* from multiple threads, then you can define ECB_NO_THREADS when compiling
1251	* libev, in which cases the memory fences become nops.	1580	* libev, in which cases the memory fences become nops.
1252	* alternatively, you can remove this #error and link against libpthread,	1581	* alternatively, you can remove this #error and link against libpthread,
1253	* which will then provide the memory fences.	1582	* which will then provide the memory fences.
1254	*/	1583	*/
1255	# error "memory fences not defined for your architecture, please report"	1584	# error "memory fences not defined for your architecture, please report"
…		…
1259	# define ECB_MEMORY_FENCE do { } while (0)	1588	# define ECB_MEMORY_FENCE do { } while (0)
1260	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE	1589	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE
1261	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	1590	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
1262	#endif	1591	#endif
1263		1592
1264	#define expect_false(cond) ecb_expect_false (cond)
1265	#define expect_true(cond) ecb_expect_true (cond)
1266	#define noinline ecb_noinline
1267
1268	#define inline_size ecb_inline	1593	#define inline_size ecb_inline
1269		1594
1270	#if EV_FEATURE_CODE	1595	#if EV_FEATURE_CODE
1271	# define inline_speed ecb_inline	1596	# define inline_speed ecb_inline
1272	#else	1597	#else
1273	# define inline_speed static noinline	1598	# define inline_speed ecb_noinline static
1274	#endif	1599	#endif
		1600
		1601	/*****************************************************************************/
		1602	/* raw syscall wrappers */
		1603
		1604	#if EV_NEED_SYSCALL
		1605
		1606	#include <sys/syscall.h>
		1607
		1608	/*
		1609	* define some syscall wrappers for common architectures
		1610	* this is mostly for nice looks during debugging, not performance.
		1611	* our syscalls return < 0, not == -1, on error. which is good
		1612	* enough for linux aio.
		1613	* TODO: arm is also common nowadays, maybe even mips and x86
		1614	* TODO: after implementing this, it suddenly looks like overkill, but its hard to remove...
		1615	*/
		1616	#if __GNUC__ && __linux && ECB_AMD64 && !defined __OPTIMIZE_SIZE__
		1617	/* the costly errno access probably kills this for size optimisation */
		1618
		1619	#define ev_syscall(nr,narg,arg1,arg2,arg3,arg4,arg5,arg6) \
		1620	({ \
		1621	long res; \
		1622	register unsigned long r6 __asm__ ("r9" ); \
		1623	register unsigned long r5 __asm__ ("r8" ); \
		1624	register unsigned long r4 __asm__ ("r10"); \
		1625	register unsigned long r3 __asm__ ("rdx"); \
		1626	register unsigned long r2 __asm__ ("rsi"); \
		1627	register unsigned long r1 __asm__ ("rdi"); \
		1628	if (narg >= 6) r6 = (unsigned long)(arg6); \
		1629	if (narg >= 5) r5 = (unsigned long)(arg5); \
		1630	if (narg >= 4) r4 = (unsigned long)(arg4); \
		1631	if (narg >= 3) r3 = (unsigned long)(arg3); \
		1632	if (narg >= 2) r2 = (unsigned long)(arg2); \
		1633	if (narg >= 1) r1 = (unsigned long)(arg1); \
		1634	__asm__ __volatile__ ( \
		1635	"syscall\n\t" \
		1636	: "=a" (res) \
		1637	: "0" (nr), "r" (r1), "r" (r2), "r" (r3), "r" (r4), "r" (r5) \
		1638	: "cc", "r11", "cx", "memory"); \
		1639	errno = -res; \
		1640	res; \
		1641	})
		1642
		1643	#endif
		1644
		1645	#ifdef ev_syscall
		1646	#define ev_syscall0(nr) ev_syscall (nr, 0, 0, 0, 0, 0, 0, 0)
		1647	#define ev_syscall1(nr,arg1) ev_syscall (nr, 1, arg1, 0, 0, 0, 0, 0)
		1648	#define ev_syscall2(nr,arg1,arg2) ev_syscall (nr, 2, arg1, arg2, 0, 0, 0, 0)
		1649	#define ev_syscall3(nr,arg1,arg2,arg3) ev_syscall (nr, 3, arg1, arg2, arg3, 0, 0, 0)
		1650	#define ev_syscall4(nr,arg1,arg2,arg3,arg4) ev_syscall (nr, 3, arg1, arg2, arg3, arg4, 0, 0)
		1651	#define ev_syscall5(nr,arg1,arg2,arg3,arg4,arg5) ev_syscall (nr, 5, arg1, arg2, arg3, arg4, arg5, 0)
		1652	#define ev_syscall6(nr,arg1,arg2,arg3,arg4,arg5,arg6) ev_syscall (nr, 6, arg1, arg2, arg3, arg4, arg5,arg6)
		1653	#else
		1654	#define ev_syscall0(nr) syscall (nr)
		1655	#define ev_syscall1(nr,arg1) syscall (nr, arg1)
		1656	#define ev_syscall2(nr,arg1,arg2) syscall (nr, arg1, arg2)
		1657	#define ev_syscall3(nr,arg1,arg2,arg3) syscall (nr, arg1, arg2, arg3)
		1658	#define ev_syscall4(nr,arg1,arg2,arg3,arg4) syscall (nr, arg1, arg2, arg3, arg4)
		1659	#define ev_syscall5(nr,arg1,arg2,arg3,arg4,arg5) syscall (nr, arg1, arg2, arg3, arg4, arg5)
		1660	#define ev_syscall6(nr,arg1,arg2,arg3,arg4,arg5,arg6) syscall (nr, arg1, arg2, arg3, arg4, arg5,arg6)
		1661	#endif
		1662
		1663	#endif
		1664
		1665	/*****************************************************************************/
1275		1666
1276	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)	1667	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)
1277		1668
1278	#if EV_MINPRI == EV_MAXPRI	1669	#if EV_MINPRI == EV_MAXPRI
1279	# define ABSPRI(w) (((W)w), 0)	1670	# define ABSPRI(w) (((W)w), 0)
1280	#else	1671	#else
1281	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)	1672	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)
1282	#endif	1673	#endif
1283		1674
1284	#define EMPTY /* required for microsofts broken pseudo-c compiler */	1675	#define EMPTY /* required for microsofts broken pseudo-c compiler */
1285	#define EMPTY2(a,b) /* used to suppress some warnings */
1286		1676
1287	typedef ev_watcher *W;	1677	typedef ev_watcher *W;
1288	typedef ev_watcher_list *WL;	1678	typedef ev_watcher_list *WL;
1289	typedef ev_watcher_time *WT;	1679	typedef ev_watcher_time *WT;
1290		1680
…		…
1315	# include "ev_win32.c"	1705	# include "ev_win32.c"
1316	#endif	1706	#endif
1317		1707
1318	/*****************************************************************************/	1708	/*****************************************************************************/
1319		1709
		1710	#if EV_USE_LINUXAIO
		1711	# include <linux/aio_abi.h> /* probably only needed for aio_context_t */
		1712	#endif
		1713
1320	/* define a suitable floor function (only used by periodics atm) */	1714	/* define a suitable floor function (only used by periodics atm) */
1321		1715
1322	#if EV_USE_FLOOR	1716	#if EV_USE_FLOOR
1323	# include <math.h>	1717	# include <math.h>
1324	# define ev_floor(v) floor (v)	1718	# define ev_floor(v) floor (v)
1325	#else	1719	#else
1326		1720
1327	#include <float.h>	1721	#include <float.h>
1328		1722
1329	/* a floor() replacement function, should be independent of ev_tstamp type */	1723	/* a floor() replacement function, should be independent of ev_tstamp type */
		1724	ecb_noinline
1330	static ev_tstamp noinline	1725	static ev_tstamp
1331	ev_floor (ev_tstamp v)	1726	ev_floor (ev_tstamp v)
1332	{	1727	{
1333	/* the choice of shift factor is not terribly important */	1728	/* the choice of shift factor is not terribly important */
1334	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */	1729	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */
1335	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;	1730	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;
1336	#else	1731	#else
1337	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;	1732	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;
1338	#endif	1733	#endif
1339		1734
		1735	/* special treatment for negative arguments */
		1736	if (ecb_expect_false (v < 0.))
		1737	{
		1738	ev_tstamp f = -ev_floor (-v);
		1739
		1740	return f - (f == v ? 0 : 1);
		1741	}
		1742
1340	/* argument too large for an unsigned long? */	1743	/* argument too large for an unsigned long? then reduce it */
1341	if (expect_false (v >= shift))	1744	if (ecb_expect_false (v >= shift))
1342	{	1745	{
1343	ev_tstamp f;	1746	ev_tstamp f;
1344		1747
1345	if (v == v - 1.)	1748	if (v == v - 1.)
1346	return v; /* very large number */	1749	return v; /* very large numbers are assumed to be integer */
1347		1750
1348	f = shift * ev_floor (v * (1. / shift));	1751	f = shift * ev_floor (v * (1. / shift));
1349	return f + ev_floor (v - f);	1752	return f + ev_floor (v - f);
1350	}	1753	}
1351		1754
1352	/* special treatment for negative args? */
1353	if (expect_false (v < 0.))
1354	{
1355	ev_tstamp f = -ev_floor (-v);
1356
1357	return f - (f == v ? 0 : 1);
1358	}
1359
1360	/* fits into an unsigned long */	1755	/* fits into an unsigned long */
1361	return (unsigned long)v;	1756	return (unsigned long)v;
1362	}	1757	}
1363		1758
1364	#endif	1759	#endif
…		…
1367		1762
1368	#ifdef __linux	1763	#ifdef __linux
1369	# include <sys/utsname.h>	1764	# include <sys/utsname.h>
1370	#endif	1765	#endif
1371		1766
1372	static unsigned int noinline ecb_cold	1767	ecb_noinline ecb_cold
		1768	static unsigned int
1373	ev_linux_version (void)	1769	ev_linux_version (void)
1374	{	1770	{
1375	#ifdef __linux	1771	#ifdef __linux
1376	unsigned int v = 0;	1772	unsigned int v = 0;
1377	struct utsname buf;	1773	struct utsname buf;
…		…
1406	}	1802	}
1407		1803
1408	/*****************************************************************************/	1804	/*****************************************************************************/
1409		1805
1410	#if EV_AVOID_STDIO	1806	#if EV_AVOID_STDIO
1411	static void noinline ecb_cold	1807	ecb_noinline ecb_cold
		1808	static void
1412	ev_printerr (const char *msg)	1809	ev_printerr (const char *msg)
1413	{	1810	{
1414	write (STDERR_FILENO, msg, strlen (msg));	1811	write (STDERR_FILENO, msg, strlen (msg));
1415	}	1812	}
1416	#endif	1813	#endif
1417		1814
1418	static void (*syserr_cb)(const char *msg) EV_THROW;	1815	static void (*syserr_cb)(const char *msg) EV_NOEXCEPT;
1419		1816
1420	void ecb_cold	1817	ecb_cold
		1818	void
1421	ev_set_syserr_cb (void (*cb)(const char *msg) EV_THROW) EV_THROW	1819	ev_set_syserr_cb (void (*cb)(const char *msg) EV_NOEXCEPT) EV_NOEXCEPT
1422	{	1820	{
1423	syserr_cb = cb;	1821	syserr_cb = cb;
1424	}	1822	}
1425		1823
1426	static void noinline ecb_cold	1824	ecb_noinline ecb_cold
		1825	static void
1427	ev_syserr (const char *msg)	1826	ev_syserr (const char *msg)
1428	{	1827	{
1429	if (!msg)	1828	if (!msg)
1430	msg = "(libev) system error";	1829	msg = "(libev) system error";
1431		1830
…		…
1444	abort ();	1843	abort ();
1445	}	1844	}
1446	}	1845	}
1447		1846
1448	static void *	1847	static void *
1449	ev_realloc_emul (void *ptr, long size) EV_THROW	1848	ev_realloc_emul (void *ptr, long size) EV_NOEXCEPT
1450	{	1849	{
1451	/* some systems, notably openbsd and darwin, fail to properly	1850	/* some systems, notably openbsd and darwin, fail to properly
1452	* implement realloc (x, 0) (as required by both ansi c-89 and	1851	* implement realloc (x, 0) (as required by both ansi c-89 and
1453	* the single unix specification, so work around them here.	1852	* the single unix specification, so work around them here.
1454	* recently, also (at least) fedora and debian started breaking it,	1853	* recently, also (at least) fedora and debian started breaking it,
…		…
1460		1859
1461	free (ptr);	1860	free (ptr);
1462	return 0;	1861	return 0;
1463	}	1862	}
1464		1863
1465	static void *(*alloc)(void *ptr, long size) EV_THROW = ev_realloc_emul;	1864	static void *(*alloc)(void *ptr, long size) EV_NOEXCEPT = ev_realloc_emul;
1466		1865
1467	void ecb_cold	1866	ecb_cold
		1867	void
1468	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_THROW) EV_THROW	1868	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_NOEXCEPT) EV_NOEXCEPT
1469	{	1869	{
1470	alloc = cb;	1870	alloc = cb;
1471	}	1871	}
1472		1872
1473	inline_speed void *	1873	inline_speed void *
…		…
1500	typedef struct	1900	typedef struct
1501	{	1901	{
1502	WL head;	1902	WL head;
1503	unsigned char events; /* the events watched for */	1903	unsigned char events; /* the events watched for */
1504	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */	1904	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */
1505	unsigned char emask; /* the epoll backend stores the actual kernel mask in here */	1905	unsigned char emask; /* some backends store the actual kernel mask in here */
1506	unsigned char unused;	1906	unsigned char eflags; /* flags field for use by backends */
1507	#if EV_USE_EPOLL	1907	#if EV_USE_EPOLL
1508	unsigned int egen; /* generation counter to counter epoll bugs */	1908	unsigned int egen; /* generation counter to counter epoll bugs */
1509	#endif	1909	#endif
1510	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP	1910	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP
1511	SOCKET handle;	1911	SOCKET handle;
…		…
1575	static int ev_default_loop_ptr;	1975	static int ev_default_loop_ptr;
1576		1976
1577	#endif	1977	#endif
1578		1978
1579	#if EV_FEATURE_API	1979	#if EV_FEATURE_API
1580	# define EV_RELEASE_CB if (expect_false (release_cb)) release_cb (EV_A)	1980	# define EV_RELEASE_CB if (ecb_expect_false (release_cb)) release_cb (EV_A)
1581	# define EV_ACQUIRE_CB if (expect_false (acquire_cb)) acquire_cb (EV_A)	1981	# define EV_ACQUIRE_CB if (ecb_expect_false (acquire_cb)) acquire_cb (EV_A)
1582	# define EV_INVOKE_PENDING invoke_cb (EV_A)	1982	# define EV_INVOKE_PENDING invoke_cb (EV_A)
1583	#else	1983	#else
1584	# define EV_RELEASE_CB (void)0	1984	# define EV_RELEASE_CB (void)0
1585	# define EV_ACQUIRE_CB (void)0	1985	# define EV_ACQUIRE_CB (void)0
1586	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)	1986	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)
…		…
1590		1990
1591	/*****************************************************************************/	1991	/*****************************************************************************/
1592		1992
1593	#ifndef EV_HAVE_EV_TIME	1993	#ifndef EV_HAVE_EV_TIME
1594	ev_tstamp	1994	ev_tstamp
1595	ev_time (void) EV_THROW	1995	ev_time (void) EV_NOEXCEPT
1596	{	1996	{
1597	#if EV_USE_REALTIME	1997	#if EV_USE_REALTIME
1598	if (expect_true (have_realtime))	1998	if (ecb_expect_true (have_realtime))
1599	{	1999	{
1600	struct timespec ts;	2000	struct timespec ts;
1601	clock_gettime (CLOCK_REALTIME, &ts);	2001	clock_gettime (CLOCK_REALTIME, &ts);
1602	return ts.tv_sec + ts.tv_nsec * 1e-9;	2002	return EV_TS_GET (ts);
1603	}	2003	}
1604	#endif	2004	#endif
1605		2005
1606	struct timeval tv;	2006	struct timeval tv;
1607	gettimeofday (&tv, 0);	2007	gettimeofday (&tv, 0);
1608	return tv.tv_sec + tv.tv_usec * 1e-6;	2008	return EV_TV_GET (tv);
1609	}	2009	}
1610	#endif	2010	#endif
1611		2011
1612	inline_size ev_tstamp	2012	inline_size ev_tstamp
1613	get_clock (void)	2013	get_clock (void)
1614	{	2014	{
1615	#if EV_USE_MONOTONIC	2015	#if EV_USE_MONOTONIC
1616	if (expect_true (have_monotonic))	2016	if (ecb_expect_true (have_monotonic))
1617	{	2017	{
1618	struct timespec ts;	2018	struct timespec ts;
1619	clock_gettime (CLOCK_MONOTONIC, &ts);	2019	clock_gettime (CLOCK_MONOTONIC, &ts);
1620	return ts.tv_sec + ts.tv_nsec * 1e-9;	2020	return EV_TS_GET (ts);
1621	}	2021	}
1622	#endif	2022	#endif
1623		2023
1624	return ev_time ();	2024	return ev_time ();
1625	}	2025	}
1626		2026
1627	#if EV_MULTIPLICITY	2027	#if EV_MULTIPLICITY
1628	ev_tstamp	2028	ev_tstamp
1629	ev_now (EV_P) EV_THROW	2029	ev_now (EV_P) EV_NOEXCEPT
1630	{	2030	{
1631	return ev_rt_now;	2031	return ev_rt_now;
1632	}	2032	}
1633	#endif	2033	#endif
1634		2034
1635	void	2035	void
1636	ev_sleep (ev_tstamp delay) EV_THROW	2036	ev_sleep (ev_tstamp delay) EV_NOEXCEPT
1637	{	2037	{
1638	if (delay > 0.)	2038	if (delay > 0.)
1639	{	2039	{
1640	#if EV_USE_NANOSLEEP	2040	#if EV_USE_NANOSLEEP
1641	struct timespec ts;	2041	struct timespec ts;
1642		2042
1643	EV_TS_SET (ts, delay);	2043	EV_TS_SET (ts, delay);
1644	nanosleep (&ts, 0);	2044	nanosleep (&ts, 0);
1645	#elif defined _WIN32	2045	#elif defined _WIN32
		2046	/* maybe this should round up, as ms is very low resolution */
		2047	/* compared to select (µs) or nanosleep (ns) */
1646	Sleep ((unsigned long)(delay * 1e3));	2048	Sleep ((unsigned long)(EV_TS_TO_MS (delay)));
1647	#else	2049	#else
1648	struct timeval tv;	2050	struct timeval tv;
1649		2051
1650	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */	2052	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */
1651	/* something not guaranteed by newer posix versions, but guaranteed */	2053	/* something not guaranteed by newer posix versions, but guaranteed */
…		…
1681	}	2083	}
1682		2084
1683	return ncur;	2085	return ncur;
1684	}	2086	}
1685		2087
1686	static void * noinline ecb_cold	2088	ecb_noinline ecb_cold
		2089	static void *
1687	array_realloc (int elem, void *base, int *cur, int cnt)	2090	array_realloc (int elem, void *base, int *cur, int cnt)
1688	{	2091	{
1689	*cur = array_nextsize (elem, *cur, cnt);	2092	*cur = array_nextsize (elem, *cur, cnt);
1690	return ev_realloc (base, elem * *cur);	2093	return ev_realloc (base, elem * *cur);
1691	}	2094	}
1692		2095
		2096	#define array_needsize_noinit(base,offset,count)
		2097
1693	#define array_init_zero(base,count) \	2098	#define array_needsize_zerofill(base,offset,count) \
1694	memset ((void *)(base), 0, sizeof (*(base)) * (count))	2099	memset ((void *)(base + offset), 0, sizeof (*(base)) * (count))
1695		2100
1696	#define array_needsize(type,base,cur,cnt,init) \	2101	#define array_needsize(type,base,cur,cnt,init) \
1697	if (expect_false ((cnt) > (cur))) \	2102	if (ecb_expect_false ((cnt) > (cur))) \
1698	{ \	2103	{ \
1699	int ecb_unused ocur_ = (cur); \	2104	ecb_unused int ocur_ = (cur); \
1700	(base) = (type *)array_realloc \	2105	(base) = (type *)array_realloc \
1701	(sizeof (type), (base), &(cur), (cnt)); \	2106	(sizeof (type), (base), &(cur), (cnt)); \
1702	init ((base) + (ocur_), (cur) - ocur_); \	2107	init ((base), ocur_, ((cur) - ocur_)); \
1703	}	2108	}
1704		2109
1705	#if 0	2110	#if 0
1706	#define array_slim(type,stem) \	2111	#define array_slim(type,stem) \
1707	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \	2112	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \
…		…
1716	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0	2121	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0
1717		2122
1718	/*****************************************************************************/	2123	/*****************************************************************************/
1719		2124
1720	/* dummy callback for pending events */	2125	/* dummy callback for pending events */
1721	static void noinline	2126	ecb_noinline
		2127	static void
1722	pendingcb (EV_P_ ev_prepare *w, int revents)	2128	pendingcb (EV_P_ ev_prepare *w, int revents)
1723	{	2129	{
1724	}	2130	}
1725		2131
1726	void noinline	2132	ecb_noinline
		2133	void
1727	ev_feed_event (EV_P_ void *w, int revents) EV_THROW	2134	ev_feed_event (EV_P_ void *w, int revents) EV_NOEXCEPT
1728	{	2135	{
1729	W w_ = (W)w;	2136	W w_ = (W)w;
1730	int pri = ABSPRI (w_);	2137	int pri = ABSPRI (w_);
1731		2138
1732	if (expect_false (w_->pending))	2139	if (ecb_expect_false (w_->pending))
1733	pendings [pri][w_->pending - 1].events |= revents;	2140	pendings [pri][w_->pending - 1].events |= revents;
1734	else	2141	else
1735	{	2142	{
1736	w_->pending = ++pendingcnt [pri];	2143	w_->pending = ++pendingcnt [pri];
1737	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, EMPTY2);	2144	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, array_needsize_noinit);
1738	pendings [pri][w_->pending - 1].w = w_;	2145	pendings [pri][w_->pending - 1].w = w_;
1739	pendings [pri][w_->pending - 1].events = revents;	2146	pendings [pri][w_->pending - 1].events = revents;
1740	}	2147	}
1741		2148
1742	pendingpri = NUMPRI - 1;	2149	pendingpri = NUMPRI - 1;
1743	}	2150	}
1744		2151
1745	inline_speed void	2152	inline_speed void
1746	feed_reverse (EV_P_ W w)	2153	feed_reverse (EV_P_ W w)
1747	{	2154	{
1748	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, EMPTY2);	2155	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, array_needsize_noinit);
1749	rfeeds [rfeedcnt++] = w;	2156	rfeeds [rfeedcnt++] = w;
1750	}	2157	}
1751		2158
1752	inline_size void	2159	inline_size void
1753	feed_reverse_done (EV_P_ int revents)	2160	feed_reverse_done (EV_P_ int revents)
…		…
1788	inline_speed void	2195	inline_speed void
1789	fd_event (EV_P_ int fd, int revents)	2196	fd_event (EV_P_ int fd, int revents)
1790	{	2197	{
1791	ANFD *anfd = anfds + fd;	2198	ANFD *anfd = anfds + fd;
1792		2199
1793	if (expect_true (!anfd->reify))	2200	if (ecb_expect_true (!anfd->reify))
1794	fd_event_nocheck (EV_A_ fd, revents);	2201	fd_event_nocheck (EV_A_ fd, revents);
1795	}	2202	}
1796		2203
1797	void	2204	void
1798	ev_feed_fd_event (EV_P_ int fd, int revents) EV_THROW	2205	ev_feed_fd_event (EV_P_ int fd, int revents) EV_NOEXCEPT
1799	{	2206	{
1800	if (fd >= 0 && fd < anfdmax)	2207	if (fd >= 0 && fd < anfdmax)
1801	fd_event_nocheck (EV_A_ fd, revents);	2208	fd_event_nocheck (EV_A_ fd, revents);
1802	}	2209	}
1803		2210
…		…
1840	ev_io *w;	2247	ev_io *w;
1841		2248
1842	unsigned char o_events = anfd->events;	2249	unsigned char o_events = anfd->events;
1843	unsigned char o_reify = anfd->reify;	2250	unsigned char o_reify = anfd->reify;
1844		2251
1845	anfd->reify = 0;	2252	anfd->reify = 0;
1846		2253
1847	/*if (expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */	2254	/*if (ecb_expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */
1848	{	2255	{
1849	anfd->events = 0;	2256	anfd->events = 0;
1850		2257
1851	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)	2258	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)
1852	anfd->events |= (unsigned char)w->events;	2259	anfd->events |= (unsigned char)w->events;
…		…
1861		2268
1862	fdchangecnt = 0;	2269	fdchangecnt = 0;
1863	}	2270	}
1864		2271
1865	/* something about the given fd changed */	2272	/* something about the given fd changed */
1866	inline_size void	2273	inline_size
		2274	void
1867	fd_change (EV_P_ int fd, int flags)	2275	fd_change (EV_P_ int fd, int flags)
1868	{	2276	{
1869	unsigned char reify = anfds [fd].reify;	2277	unsigned char reify = anfds [fd].reify;
1870	anfds [fd].reify |= flags;	2278	anfds [fd].reify |= flags;
1871		2279
1872	if (expect_true (!reify))	2280	if (ecb_expect_true (!reify))
1873	{	2281	{
1874	++fdchangecnt;	2282	++fdchangecnt;
1875	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, EMPTY2);	2283	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, array_needsize_noinit);
1876	fdchanges [fdchangecnt - 1] = fd;	2284	fdchanges [fdchangecnt - 1] = fd;
1877	}	2285	}
1878	}	2286	}
1879		2287
1880	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */	2288	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */
1881	inline_speed void ecb_cold	2289	inline_speed ecb_cold void
1882	fd_kill (EV_P_ int fd)	2290	fd_kill (EV_P_ int fd)
1883	{	2291	{
1884	ev_io *w;	2292	ev_io *w;
1885		2293
1886	while ((w = (ev_io *)anfds [fd].head))	2294	while ((w = (ev_io *)anfds [fd].head))
…		…
1889	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);	2297	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);
1890	}	2298	}
1891	}	2299	}
1892		2300
1893	/* check whether the given fd is actually valid, for error recovery */	2301	/* check whether the given fd is actually valid, for error recovery */
1894	inline_size int ecb_cold	2302	inline_size ecb_cold int
1895	fd_valid (int fd)	2303	fd_valid (int fd)
1896	{	2304	{
1897	#ifdef _WIN32	2305	#ifdef _WIN32
1898	return EV_FD_TO_WIN32_HANDLE (fd) != -1;	2306	return EV_FD_TO_WIN32_HANDLE (fd) != -1;
1899	#else	2307	#else
1900	return fcntl (fd, F_GETFD) != -1;	2308	return fcntl (fd, F_GETFD) != -1;
1901	#endif	2309	#endif
1902	}	2310	}
1903		2311
1904	/* called on EBADF to verify fds */	2312	/* called on EBADF to verify fds */
1905	static void noinline ecb_cold	2313	ecb_noinline ecb_cold
		2314	static void
1906	fd_ebadf (EV_P)	2315	fd_ebadf (EV_P)
1907	{	2316	{
1908	int fd;	2317	int fd;
1909		2318
1910	for (fd = 0; fd < anfdmax; ++fd)	2319	for (fd = 0; fd < anfdmax; ++fd)
…		…
1912	if (!fd_valid (fd) && errno == EBADF)	2321	if (!fd_valid (fd) && errno == EBADF)
1913	fd_kill (EV_A_ fd);	2322	fd_kill (EV_A_ fd);
1914	}	2323	}
1915		2324
1916	/* called on ENOMEM in select/poll to kill some fds and retry */	2325	/* called on ENOMEM in select/poll to kill some fds and retry */
1917	static void noinline ecb_cold	2326	ecb_noinline ecb_cold
		2327	static void
1918	fd_enomem (EV_P)	2328	fd_enomem (EV_P)
1919	{	2329	{
1920	int fd;	2330	int fd;
1921		2331
1922	for (fd = anfdmax; fd--; )	2332	for (fd = anfdmax; fd--; )
…		…
1926	break;	2336	break;
1927	}	2337	}
1928	}	2338	}
1929		2339
1930	/* usually called after fork if backend needs to re-arm all fds from scratch */	2340	/* usually called after fork if backend needs to re-arm all fds from scratch */
1931	static void noinline	2341	ecb_noinline
		2342	static void
1932	fd_rearm_all (EV_P)	2343	fd_rearm_all (EV_P)
1933	{	2344	{
1934	int fd;	2345	int fd;
1935		2346
1936	for (fd = 0; fd < anfdmax; ++fd)	2347	for (fd = 0; fd < anfdmax; ++fd)
…		…
1989	ev_tstamp minat;	2400	ev_tstamp minat;
1990	ANHE *minpos;	2401	ANHE *minpos;
1991	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;	2402	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;
1992		2403
1993	/* find minimum child */	2404	/* find minimum child */
1994	if (expect_true (pos + DHEAP - 1 < E))	2405	if (ecb_expect_true (pos + DHEAP - 1 < E))
1995	{	2406	{
1996	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));	2407	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));
1997	if ( ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));	2408	if ( minat > ANHE_at (pos [1])) (minpos = pos + 1), (minat = ANHE_at (*minpos));
1998	if ( ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));	2409	if ( minat > ANHE_at (pos [2])) (minpos = pos + 2), (minat = ANHE_at (*minpos));
1999	if ( ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));	2410	if ( minat > ANHE_at (pos [3])) (minpos = pos + 3), (minat = ANHE_at (*minpos));
2000	}	2411	}
2001	else if (pos < E)	2412	else if (pos < E)
2002	{	2413	{
2003	/* slow path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));	2414	/* slow path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));
2004	if (pos + 1 < E && ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));	2415	if (pos + 1 < E && minat > ANHE_at (pos [1])) (minpos = pos + 1), (minat = ANHE_at (*minpos));
2005	if (pos + 2 < E && ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));	2416	if (pos + 2 < E && minat > ANHE_at (pos [2])) (minpos = pos + 2), (minat = ANHE_at (*minpos));
2006	if (pos + 3 < E && ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));	2417	if (pos + 3 < E && minat > ANHE_at (pos [3])) (minpos = pos + 3), (minat = ANHE_at (*minpos));
2007	}	2418	}
2008	else	2419	else
2009	break;	2420	break;
2010		2421
2011	if (ANHE_at (he) <= minat)	2422	if (ANHE_at (he) <= minat)
…		…
2019		2430
2020	heap [k] = he;	2431	heap [k] = he;
2021	ev_active (ANHE_w (he)) = k;	2432	ev_active (ANHE_w (he)) = k;
2022	}	2433	}
2023		2434
2024	#else /* 4HEAP */	2435	#else /* not 4HEAP */
2025		2436
2026	#define HEAP0 1	2437	#define HEAP0 1
2027	#define HPARENT(k) ((k) >> 1)	2438	#define HPARENT(k) ((k) >> 1)
2028	#define UPHEAP_DONE(p,k) (!(p))	2439	#define UPHEAP_DONE(p,k) (!(p))
2029		2440
…		…
2117		2528
2118	/*****************************************************************************/	2529	/*****************************************************************************/
2119		2530
2120	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	2531	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2121		2532
2122	static void noinline ecb_cold	2533	ecb_noinline ecb_cold
		2534	static void
2123	evpipe_init (EV_P)	2535	evpipe_init (EV_P)
2124	{	2536	{
2125	if (!ev_is_active (&pipe_w))	2537	if (!ev_is_active (&pipe_w))
2126	{	2538	{
2127	int fds [2];	2539	int fds [2];
…		…
2167	inline_speed void	2579	inline_speed void
2168	evpipe_write (EV_P_ EV_ATOMIC_T *flag)	2580	evpipe_write (EV_P_ EV_ATOMIC_T *flag)
2169	{	2581	{
2170	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */	2582	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */
2171		2583
2172	if (expect_true (*flag))	2584	if (ecb_expect_true (*flag))
2173	return;	2585	return;
2174		2586
2175	*flag = 1;	2587	*flag = 1;
2176	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */	2588	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */
2177		2589
…		…
2198	#endif	2610	#endif
2199	{	2611	{
2200	#ifdef _WIN32	2612	#ifdef _WIN32
2201	WSABUF buf;	2613	WSABUF buf;
2202	DWORD sent;	2614	DWORD sent;
2203	buf.buf = &buf;	2615	buf.buf = (char *)&buf;
2204	buf.len = 1;	2616	buf.len = 1;
2205	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);	2617	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);
2206	#else	2618	#else
2207	write (evpipe [1], &(evpipe [1]), 1);	2619	write (evpipe [1], &(evpipe [1]), 1);
2208	#endif	2620	#endif
…		…
2254	sig_pending = 0;	2666	sig_pending = 0;
2255		2667
2256	ECB_MEMORY_FENCE;	2668	ECB_MEMORY_FENCE;
2257		2669
2258	for (i = EV_NSIG - 1; i--; )	2670	for (i = EV_NSIG - 1; i--; )
2259	if (expect_false (signals [i].pending))	2671	if (ecb_expect_false (signals [i].pending))
2260	ev_feed_signal_event (EV_A_ i + 1);	2672	ev_feed_signal_event (EV_A_ i + 1);
2261	}	2673	}
2262	#endif	2674	#endif
2263		2675
2264	#if EV_ASYNC_ENABLE	2676	#if EV_ASYNC_ENABLE
…		…
2280	}	2692	}
2281		2693
2282	/*****************************************************************************/	2694	/*****************************************************************************/
2283		2695
2284	void	2696	void
2285	ev_feed_signal (int signum) EV_THROW	2697	ev_feed_signal (int signum) EV_NOEXCEPT
2286	{	2698	{
2287	#if EV_MULTIPLICITY	2699	#if EV_MULTIPLICITY
2288	EV_P;	2700	EV_P;
2289	ECB_MEMORY_FENCE_ACQUIRE;	2701	ECB_MEMORY_FENCE_ACQUIRE;
2290	EV_A = signals [signum - 1].loop;	2702	EV_A = signals [signum - 1].loop;
…		…
2305	#endif	2717	#endif
2306		2718
2307	ev_feed_signal (signum);	2719	ev_feed_signal (signum);
2308	}	2720	}
2309		2721
2310	void noinline	2722	ecb_noinline
		2723	void
2311	ev_feed_signal_event (EV_P_ int signum) EV_THROW	2724	ev_feed_signal_event (EV_P_ int signum) EV_NOEXCEPT
2312	{	2725	{
2313	WL w;	2726	WL w;
2314		2727
2315	if (expect_false (signum <= 0 || signum >= EV_NSIG))	2728	if (ecb_expect_false (signum <= 0 || signum >= EV_NSIG))
2316	return;	2729	return;
2317		2730
2318	--signum;	2731	--signum;
2319		2732
2320	#if EV_MULTIPLICITY	2733	#if EV_MULTIPLICITY
2321	/* it is permissible to try to feed a signal to the wrong loop */	2734	/* it is permissible to try to feed a signal to the wrong loop */
2322	/* or, likely more useful, feeding a signal nobody is waiting for */	2735	/* or, likely more useful, feeding a signal nobody is waiting for */
2323		2736
2324	if (expect_false (signals [signum].loop != EV_A))	2737	if (ecb_expect_false (signals [signum].loop != EV_A))
2325	return;	2738	return;
2326	#endif	2739	#endif
2327		2740
2328	signals [signum].pending = 0;	2741	signals [signum].pending = 0;
2329	ECB_MEMORY_FENCE_RELEASE;	2742	ECB_MEMORY_FENCE_RELEASE;
…		…
2425	# include "ev_kqueue.c"	2838	# include "ev_kqueue.c"
2426	#endif	2839	#endif
2427	#if EV_USE_EPOLL	2840	#if EV_USE_EPOLL
2428	# include "ev_epoll.c"	2841	# include "ev_epoll.c"
2429	#endif	2842	#endif
		2843	#if EV_USE_LINUXAIO
		2844	# include "ev_linuxaio.c"
		2845	#endif
		2846	#if EV_USE_IOURING
		2847	# include "ev_iouring.c"
		2848	#endif
2430	#if EV_USE_POLL	2849	#if EV_USE_POLL
2431	# include "ev_poll.c"	2850	# include "ev_poll.c"
2432	#endif	2851	#endif
2433	#if EV_USE_SELECT	2852	#if EV_USE_SELECT
2434	# include "ev_select.c"	2853	# include "ev_select.c"
2435	#endif	2854	#endif
2436		2855
2437	int ecb_cold	2856	ecb_cold int
2438	ev_version_major (void) EV_THROW	2857	ev_version_major (void) EV_NOEXCEPT
2439	{	2858	{
2440	return EV_VERSION_MAJOR;	2859	return EV_VERSION_MAJOR;
2441	}	2860	}
2442		2861
2443	int ecb_cold	2862	ecb_cold int
2444	ev_version_minor (void) EV_THROW	2863	ev_version_minor (void) EV_NOEXCEPT
2445	{	2864	{
2446	return EV_VERSION_MINOR;	2865	return EV_VERSION_MINOR;
2447	}	2866	}
2448		2867
2449	/* return true if we are running with elevated privileges and should ignore env variables */	2868	/* return true if we are running with elevated privileges and should ignore env variables */
2450	int inline_size ecb_cold	2869	inline_size ecb_cold int
2451	enable_secure (void)	2870	enable_secure (void)
2452	{	2871	{
2453	#ifdef _WIN32	2872	#ifdef _WIN32
2454	return 0;	2873	return 0;
2455	#else	2874	#else
2456	return getuid () != geteuid ()	2875	return getuid () != geteuid ()
2457	|| getgid () != getegid ();	2876	|| getgid () != getegid ();
2458	#endif	2877	#endif
2459	}	2878	}
2460		2879
2461	unsigned int ecb_cold	2880	ecb_cold
		2881	unsigned int
2462	ev_supported_backends (void) EV_THROW	2882	ev_supported_backends (void) EV_NOEXCEPT
2463	{	2883	{
2464	unsigned int flags = 0;	2884	unsigned int flags = 0;
2465		2885
2466	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;	2886	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;
2467	if (EV_USE_KQUEUE) flags |= EVBACKEND_KQUEUE;	2887	if (EV_USE_KQUEUE ) flags |= EVBACKEND_KQUEUE;
2468	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;	2888	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;
		2889	if (EV_USE_LINUXAIO) flags |= EVBACKEND_LINUXAIO;
		2890	if (EV_USE_IOURING ) flags |= EVBACKEND_IOURING;
2469	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;	2891	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;
2470	if (EV_USE_SELECT) flags |= EVBACKEND_SELECT;	2892	if (EV_USE_SELECT ) flags |= EVBACKEND_SELECT;
2471		2893
2472	return flags;	2894	return flags;
2473	}	2895	}
2474		2896
2475	unsigned int ecb_cold	2897	ecb_cold
		2898	unsigned int
2476	ev_recommended_backends (void) EV_THROW	2899	ev_recommended_backends (void) EV_NOEXCEPT
2477	{	2900	{
2478	unsigned int flags = ev_supported_backends ();	2901	unsigned int flags = ev_supported_backends ();
2479		2902
2480	#ifndef __NetBSD__	2903	#ifndef __NetBSD__
2481	/* kqueue is borked on everything but netbsd apparently */	2904	/* kqueue is borked on everything but netbsd apparently */
…		…
2489	#endif	2912	#endif
2490	#ifdef __FreeBSD__	2913	#ifdef __FreeBSD__
2491	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */	2914	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */
2492	#endif	2915	#endif
2493		2916
		2917	/* TODO: linuxaio is very experimental */
		2918	#if !EV_RECOMMEND_LINUXAIO
		2919	flags &= ~EVBACKEND_LINUXAIO;
		2920	#endif
		2921	/* TODO: linuxaio is super experimental */
		2922	#if !EV_RECOMMEND_IOURING
		2923	flags &= ~EVBACKEND_IOURING;
		2924	#endif
		2925
2494	return flags;	2926	return flags;
2495	}	2927	}
2496		2928
2497	unsigned int ecb_cold	2929	ecb_cold
		2930	unsigned int
2498	ev_embeddable_backends (void) EV_THROW	2931	ev_embeddable_backends (void) EV_NOEXCEPT
2499	{	2932	{
2500	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;	2933	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;
2501		2934
2502	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */	2935	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */
2503	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */	2936	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */
2504	flags &= ~EVBACKEND_EPOLL;	2937	flags &= ~EVBACKEND_EPOLL;
2505		2938
		2939	/* EVBACKEND_LINUXAIO is theoretically embeddable, but suffers from a performance overhead */
		2940
		2941	/* EVBACKEND_IOURING is practically embeddable, but the current implementation is not
		2942	* because our backend_fd is the epoll fd we need as fallback.
		2943	* if the kernel ever is fixed, this might change...
		2944	*/
		2945
2506	return flags;	2946	return flags;
2507	}	2947	}
2508		2948
2509	unsigned int	2949	unsigned int
2510	ev_backend (EV_P) EV_THROW	2950	ev_backend (EV_P) EV_NOEXCEPT
2511	{	2951	{
2512	return backend;	2952	return backend;
2513	}	2953	}
2514		2954
2515	#if EV_FEATURE_API	2955	#if EV_FEATURE_API
2516	unsigned int	2956	unsigned int
2517	ev_iteration (EV_P) EV_THROW	2957	ev_iteration (EV_P) EV_NOEXCEPT
2518	{	2958	{
2519	return loop_count;	2959	return loop_count;
2520	}	2960	}
2521		2961
2522	unsigned int	2962	unsigned int
2523	ev_depth (EV_P) EV_THROW	2963	ev_depth (EV_P) EV_NOEXCEPT
2524	{	2964	{
2525	return loop_depth;	2965	return loop_depth;
2526	}	2966	}
2527		2967
2528	void	2968	void
2529	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2969	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2530	{	2970	{
2531	io_blocktime = interval;	2971	io_blocktime = interval;
2532	}	2972	}
2533		2973
2534	void	2974	void
2535	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2975	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2536	{	2976	{
2537	timeout_blocktime = interval;	2977	timeout_blocktime = interval;
2538	}	2978	}
2539		2979
2540	void	2980	void
2541	ev_set_userdata (EV_P_ void *data) EV_THROW	2981	ev_set_userdata (EV_P_ void *data) EV_NOEXCEPT
2542	{	2982	{
2543	userdata = data;	2983	userdata = data;
2544	}	2984	}
2545		2985
2546	void *	2986	void *
2547	ev_userdata (EV_P) EV_THROW	2987	ev_userdata (EV_P) EV_NOEXCEPT
2548	{	2988	{
2549	return userdata;	2989	return userdata;
2550	}	2990	}
2551		2991
2552	void	2992	void
2553	ev_set_invoke_pending_cb (EV_P_ void (*invoke_pending_cb)(EV_P)) EV_THROW	2993	ev_set_invoke_pending_cb (EV_P_ ev_loop_callback invoke_pending_cb) EV_NOEXCEPT
2554	{	2994	{
2555	invoke_cb = invoke_pending_cb;	2995	invoke_cb = invoke_pending_cb;
2556	}	2996	}
2557		2997
2558	void	2998	void
2559	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_THROW, void (*acquire)(EV_P) EV_THROW) EV_THROW	2999	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_NOEXCEPT, void (*acquire)(EV_P) EV_NOEXCEPT) EV_NOEXCEPT
2560	{	3000	{
2561	release_cb = release;	3001	release_cb = release;
2562	acquire_cb = acquire;	3002	acquire_cb = acquire;
2563	}	3003	}
2564	#endif	3004	#endif
2565		3005
2566	/* initialise a loop structure, must be zero-initialised */	3006	/* initialise a loop structure, must be zero-initialised */
2567	static void noinline ecb_cold	3007	ecb_noinline ecb_cold
		3008	static void
2568	loop_init (EV_P_ unsigned int flags) EV_THROW	3009	loop_init (EV_P_ unsigned int flags) EV_NOEXCEPT
2569	{	3010	{
2570	if (!backend)	3011	if (!backend)
2571	{	3012	{
2572	origflags = flags;	3013	origflags = flags;
2573		3014
…		…
2631		3072
2632	if (!(flags & EVBACKEND_MASK))	3073	if (!(flags & EVBACKEND_MASK))
2633	flags |= ev_recommended_backends ();	3074	flags |= ev_recommended_backends ();
2634		3075
2635	#if EV_USE_IOCP	3076	#if EV_USE_IOCP
2636	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);	3077	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);
2637	#endif	3078	#endif
2638	#if EV_USE_PORT	3079	#if EV_USE_PORT
2639	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);	3080	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);
2640	#endif	3081	#endif
2641	#if EV_USE_KQUEUE	3082	#if EV_USE_KQUEUE
2642	if (!backend && (flags & EVBACKEND_KQUEUE)) backend = kqueue_init (EV_A_ flags);	3083	if (!backend && (flags & EVBACKEND_KQUEUE )) backend = kqueue_init (EV_A_ flags);
		3084	#endif
		3085	#if EV_USE_IOURING
		3086	if (!backend && (flags & EVBACKEND_IOURING )) backend = iouring_init (EV_A_ flags);
		3087	#endif
		3088	#if EV_USE_LINUXAIO
		3089	if (!backend && (flags & EVBACKEND_LINUXAIO)) backend = linuxaio_init (EV_A_ flags);
2643	#endif	3090	#endif
2644	#if EV_USE_EPOLL	3091	#if EV_USE_EPOLL
2645	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);	3092	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);
2646	#endif	3093	#endif
2647	#if EV_USE_POLL	3094	#if EV_USE_POLL
2648	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);	3095	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);
2649	#endif	3096	#endif
2650	#if EV_USE_SELECT	3097	#if EV_USE_SELECT
2651	if (!backend && (flags & EVBACKEND_SELECT)) backend = select_init (EV_A_ flags);	3098	if (!backend && (flags & EVBACKEND_SELECT )) backend = select_init (EV_A_ flags);
2652	#endif	3099	#endif
2653		3100
2654	ev_prepare_init (&pending_w, pendingcb);	3101	ev_prepare_init (&pending_w, pendingcb);
2655		3102
2656	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	3103	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
…		…
2659	#endif	3106	#endif
2660	}	3107	}
2661	}	3108	}
2662		3109
2663	/* free up a loop structure */	3110	/* free up a loop structure */
2664	void ecb_cold	3111	ecb_cold
		3112	void
2665	ev_loop_destroy (EV_P)	3113	ev_loop_destroy (EV_P)
2666	{	3114	{
2667	int i;	3115	int i;
2668		3116
2669	#if EV_MULTIPLICITY	3117	#if EV_MULTIPLICITY
…		…
2672	return;	3120	return;
2673	#endif	3121	#endif
2674		3122
2675	#if EV_CLEANUP_ENABLE	3123	#if EV_CLEANUP_ENABLE
2676	/* queue cleanup watchers (and execute them) */	3124	/* queue cleanup watchers (and execute them) */
2677	if (expect_false (cleanupcnt))	3125	if (ecb_expect_false (cleanupcnt))
2678	{	3126	{
2679	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);	3127	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);
2680	EV_INVOKE_PENDING;	3128	EV_INVOKE_PENDING;
2681	}	3129	}
2682	#endif	3130	#endif
…		…
2710		3158
2711	if (backend_fd >= 0)	3159	if (backend_fd >= 0)
2712	close (backend_fd);	3160	close (backend_fd);
2713		3161
2714	#if EV_USE_IOCP	3162	#if EV_USE_IOCP
2715	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);	3163	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);
2716	#endif	3164	#endif
2717	#if EV_USE_PORT	3165	#if EV_USE_PORT
2718	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);	3166	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);
2719	#endif	3167	#endif
2720	#if EV_USE_KQUEUE	3168	#if EV_USE_KQUEUE
2721	if (backend == EVBACKEND_KQUEUE) kqueue_destroy (EV_A);	3169	if (backend == EVBACKEND_KQUEUE ) kqueue_destroy (EV_A);
		3170	#endif
		3171	#if EV_USE_IOURING
		3172	if (backend == EVBACKEND_IOURING ) iouring_destroy (EV_A);
		3173	#endif
		3174	#if EV_USE_LINUXAIO
		3175	if (backend == EVBACKEND_LINUXAIO) linuxaio_destroy (EV_A);
2722	#endif	3176	#endif
2723	#if EV_USE_EPOLL	3177	#if EV_USE_EPOLL
2724	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);	3178	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);
2725	#endif	3179	#endif
2726	#if EV_USE_POLL	3180	#if EV_USE_POLL
2727	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);	3181	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);
2728	#endif	3182	#endif
2729	#if EV_USE_SELECT	3183	#if EV_USE_SELECT
2730	if (backend == EVBACKEND_SELECT) select_destroy (EV_A);	3184	if (backend == EVBACKEND_SELECT ) select_destroy (EV_A);
2731	#endif	3185	#endif
2732		3186
2733	for (i = NUMPRI; i--; )	3187	for (i = NUMPRI; i--; )
2734	{	3188	{
2735	array_free (pending, [i]);	3189	array_free (pending, [i]);
…		…
2777		3231
2778	inline_size void	3232	inline_size void
2779	loop_fork (EV_P)	3233	loop_fork (EV_P)
2780	{	3234	{
2781	#if EV_USE_PORT	3235	#if EV_USE_PORT
2782	if (backend == EVBACKEND_PORT ) port_fork (EV_A);	3236	if (backend == EVBACKEND_PORT ) port_fork (EV_A);
2783	#endif	3237	#endif
2784	#if EV_USE_KQUEUE	3238	#if EV_USE_KQUEUE
2785	if (backend == EVBACKEND_KQUEUE) kqueue_fork (EV_A);	3239	if (backend == EVBACKEND_KQUEUE ) kqueue_fork (EV_A);
		3240	#endif
		3241	#if EV_USE_IOURING
		3242	if (backend == EVBACKEND_IOURING ) iouring_fork (EV_A);
		3243	#endif
		3244	#if EV_USE_LINUXAIO
		3245	if (backend == EVBACKEND_LINUXAIO) linuxaio_fork (EV_A);
2786	#endif	3246	#endif
2787	#if EV_USE_EPOLL	3247	#if EV_USE_EPOLL
2788	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);	3248	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);
2789	#endif	3249	#endif
2790	#if EV_USE_INOTIFY	3250	#if EV_USE_INOTIFY
2791	infy_fork (EV_A);	3251	infy_fork (EV_A);
2792	#endif	3252	#endif
2793		3253
2794	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	3254	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2795	if (ev_is_active (&pipe_w))	3255	if (ev_is_active (&pipe_w) && postfork != 2)
2796	{	3256	{
2797	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */	3257	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */
2798		3258
2799	ev_ref (EV_A);	3259	ev_ref (EV_A);
2800	ev_io_stop (EV_A_ &pipe_w);	3260	ev_io_stop (EV_A_ &pipe_w);
…		…
2811	postfork = 0;	3271	postfork = 0;
2812	}	3272	}
2813		3273
2814	#if EV_MULTIPLICITY	3274	#if EV_MULTIPLICITY
2815		3275
		3276	ecb_cold
2816	struct ev_loop * ecb_cold	3277	struct ev_loop *
2817	ev_loop_new (unsigned int flags) EV_THROW	3278	ev_loop_new (unsigned int flags) EV_NOEXCEPT
2818	{	3279	{
2819	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));	3280	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));
2820		3281
2821	memset (EV_A, 0, sizeof (struct ev_loop));	3282	memset (EV_A, 0, sizeof (struct ev_loop));
2822	loop_init (EV_A_ flags);	3283	loop_init (EV_A_ flags);
…		…
2829	}	3290	}
2830		3291
2831	#endif /* multiplicity */	3292	#endif /* multiplicity */
2832		3293
2833	#if EV_VERIFY	3294	#if EV_VERIFY
2834	static void noinline ecb_cold	3295	ecb_noinline ecb_cold
		3296	static void
2835	verify_watcher (EV_P_ W w)	3297	verify_watcher (EV_P_ W w)
2836	{	3298	{
2837	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));	3299	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));
2838		3300
2839	if (w->pending)	3301	if (w->pending)
2840	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));	3302	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));
2841	}	3303	}
2842		3304
2843	static void noinline ecb_cold	3305	ecb_noinline ecb_cold
		3306	static void
2844	verify_heap (EV_P_ ANHE *heap, int N)	3307	verify_heap (EV_P_ ANHE *heap, int N)
2845	{	3308	{
2846	int i;	3309	int i;
2847		3310
2848	for (i = HEAP0; i < N + HEAP0; ++i)	3311	for (i = HEAP0; i < N + HEAP0; ++i)
…		…
2853		3316
2854	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));	3317	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));
2855	}	3318	}
2856	}	3319	}
2857		3320
2858	static void noinline ecb_cold	3321	ecb_noinline ecb_cold
		3322	static void
2859	array_verify (EV_P_ W *ws, int cnt)	3323	array_verify (EV_P_ W *ws, int cnt)
2860	{	3324	{
2861	while (cnt--)	3325	while (cnt--)
2862	{	3326	{
2863	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));	3327	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));
…		…
2866	}	3330	}
2867	#endif	3331	#endif
2868		3332
2869	#if EV_FEATURE_API	3333	#if EV_FEATURE_API
2870	void ecb_cold	3334	void ecb_cold
2871	ev_verify (EV_P) EV_THROW	3335	ev_verify (EV_P) EV_NOEXCEPT
2872	{	3336	{
2873	#if EV_VERIFY	3337	#if EV_VERIFY
2874	int i;	3338	int i;
2875	WL w, w2;	3339	WL w, w2;
2876		3340
…		…
2952	#endif	3416	#endif
2953	}	3417	}
2954	#endif	3418	#endif
2955		3419
2956	#if EV_MULTIPLICITY	3420	#if EV_MULTIPLICITY
		3421	ecb_cold
2957	struct ev_loop * ecb_cold	3422	struct ev_loop *
2958	#else	3423	#else
2959	int	3424	int
2960	#endif	3425	#endif
2961	ev_default_loop (unsigned int flags) EV_THROW	3426	ev_default_loop (unsigned int flags) EV_NOEXCEPT
2962	{	3427	{
2963	if (!ev_default_loop_ptr)	3428	if (!ev_default_loop_ptr)
2964	{	3429	{
2965	#if EV_MULTIPLICITY	3430	#if EV_MULTIPLICITY
2966	EV_P = ev_default_loop_ptr = &default_loop_struct;	3431	EV_P = ev_default_loop_ptr = &default_loop_struct;
…		…
2985		3450
2986	return ev_default_loop_ptr;	3451	return ev_default_loop_ptr;
2987	}	3452	}
2988		3453
2989	void	3454	void
2990	ev_loop_fork (EV_P) EV_THROW	3455	ev_loop_fork (EV_P) EV_NOEXCEPT
2991	{	3456	{
2992	postfork = 1;	3457	postfork = 1;
2993	}	3458	}
2994		3459
2995	/*****************************************************************************/	3460	/*****************************************************************************/
…		…
2999	{	3464	{
3000	EV_CB_INVOKE ((W)w, revents);	3465	EV_CB_INVOKE ((W)w, revents);
3001	}	3466	}
3002		3467
3003	unsigned int	3468	unsigned int
3004	ev_pending_count (EV_P) EV_THROW	3469	ev_pending_count (EV_P) EV_NOEXCEPT
3005	{	3470	{
3006	int pri;	3471	int pri;
3007	unsigned int count = 0;	3472	unsigned int count = 0;
3008		3473
3009	for (pri = NUMPRI; pri--; )	3474	for (pri = NUMPRI; pri--; )
3010	count += pendingcnt [pri];	3475	count += pendingcnt [pri];
3011		3476
3012	return count;	3477	return count;
3013	}	3478	}
3014		3479
3015	void noinline	3480	ecb_noinline
		3481	void
3016	ev_invoke_pending (EV_P)	3482	ev_invoke_pending (EV_P)
3017	{	3483	{
3018	pendingpri = NUMPRI;	3484	pendingpri = NUMPRI;
3019		3485
3020	while (pendingpri) /* pendingpri possibly gets modified in the inner loop */	3486	do
3021	{	3487	{
3022	--pendingpri;	3488	--pendingpri;
3023		3489
		3490	/* pendingpri possibly gets modified in the inner loop */
3024	while (pendingcnt [pendingpri])	3491	while (pendingcnt [pendingpri])
3025	{	3492	{
3026	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];	3493	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];
3027		3494
3028	p->w->pending = 0;	3495	p->w->pending = 0;
3029	EV_CB_INVOKE (p->w, p->events);	3496	EV_CB_INVOKE (p->w, p->events);
3030	EV_FREQUENT_CHECK;	3497	EV_FREQUENT_CHECK;
3031	}	3498	}
3032	}	3499	}
		3500	while (pendingpri);
3033	}	3501	}
3034		3502
3035	#if EV_IDLE_ENABLE	3503	#if EV_IDLE_ENABLE
3036	/* make idle watchers pending. this handles the "call-idle */	3504	/* make idle watchers pending. this handles the "call-idle */
3037	/* only when higher priorities are idle" logic */	3505	/* only when higher priorities are idle" logic */
3038	inline_size void	3506	inline_size void
3039	idle_reify (EV_P)	3507	idle_reify (EV_P)
3040	{	3508	{
3041	if (expect_false (idleall))	3509	if (ecb_expect_false (idleall))
3042	{	3510	{
3043	int pri;	3511	int pri;
3044		3512
3045	for (pri = NUMPRI; pri--; )	3513	for (pri = NUMPRI; pri--; )
3046	{	3514	{
…		…
3095	}	3563	}
3096	}	3564	}
3097		3565
3098	#if EV_PERIODIC_ENABLE	3566	#if EV_PERIODIC_ENABLE
3099		3567
3100	static void noinline	3568	ecb_noinline
		3569	static void
3101	periodic_recalc (EV_P_ ev_periodic *w)	3570	periodic_recalc (EV_P_ ev_periodic *w)
3102	{	3571	{
3103	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;	3572	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;
3104	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);	3573	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);
3105		3574
…		…
3107	while (at <= ev_rt_now)	3576	while (at <= ev_rt_now)
3108	{	3577	{
3109	ev_tstamp nat = at + w->interval;	3578	ev_tstamp nat = at + w->interval;
3110		3579
3111	/* when resolution fails us, we use ev_rt_now */	3580	/* when resolution fails us, we use ev_rt_now */
3112	if (expect_false (nat == at))	3581	if (ecb_expect_false (nat == at))
3113	{	3582	{
3114	at = ev_rt_now;	3583	at = ev_rt_now;
3115	break;	3584	break;
3116	}	3585	}
3117		3586
…		…
3163	}	3632	}
3164	}	3633	}
3165		3634
3166	/* simply recalculate all periodics */	3635	/* simply recalculate all periodics */
3167	/* TODO: maybe ensure that at least one event happens when jumping forward? */	3636	/* TODO: maybe ensure that at least one event happens when jumping forward? */
3168	static void noinline ecb_cold	3637	ecb_noinline ecb_cold
		3638	static void
3169	periodics_reschedule (EV_P)	3639	periodics_reschedule (EV_P)
3170	{	3640	{
3171	int i;	3641	int i;
3172		3642
3173	/* adjust periodics after time jump */	3643	/* adjust periodics after time jump */
…		…
3186	reheap (periodics, periodiccnt);	3656	reheap (periodics, periodiccnt);
3187	}	3657	}
3188	#endif	3658	#endif
3189		3659
3190	/* adjust all timers by a given offset */	3660	/* adjust all timers by a given offset */
3191	static void noinline ecb_cold	3661	ecb_noinline ecb_cold
		3662	static void
3192	timers_reschedule (EV_P_ ev_tstamp adjust)	3663	timers_reschedule (EV_P_ ev_tstamp adjust)
3193	{	3664	{
3194	int i;	3665	int i;
3195		3666
3196	for (i = 0; i < timercnt; ++i)	3667	for (i = 0; i < timercnt; ++i)
…		…
3205	/* also detect if there was a timejump, and act accordingly */	3676	/* also detect if there was a timejump, and act accordingly */
3206	inline_speed void	3677	inline_speed void
3207	time_update (EV_P_ ev_tstamp max_block)	3678	time_update (EV_P_ ev_tstamp max_block)
3208	{	3679	{
3209	#if EV_USE_MONOTONIC	3680	#if EV_USE_MONOTONIC
3210	if (expect_true (have_monotonic))	3681	if (ecb_expect_true (have_monotonic))
3211	{	3682	{
3212	int i;	3683	int i;
3213	ev_tstamp odiff = rtmn_diff;	3684	ev_tstamp odiff = rtmn_diff;
3214		3685
3215	mn_now = get_clock ();	3686	mn_now = get_clock ();
3216		3687
3217	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */	3688	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */
3218	/* interpolate in the meantime */	3689	/* interpolate in the meantime */
3219	if (expect_true (mn_now - now_floor < MIN_TIMEJUMP * .5))	3690	if (ecb_expect_true (mn_now - now_floor < MIN_TIMEJUMP * .5))
3220	{	3691	{
3221	ev_rt_now = rtmn_diff + mn_now;	3692	ev_rt_now = rtmn_diff + mn_now;
3222	return;	3693	return;
3223	}	3694	}
3224		3695
…		…
3238	ev_tstamp diff;	3709	ev_tstamp diff;
3239	rtmn_diff = ev_rt_now - mn_now;	3710	rtmn_diff = ev_rt_now - mn_now;
3240		3711
3241	diff = odiff - rtmn_diff;	3712	diff = odiff - rtmn_diff;
3242		3713
3243	if (expect_true ((diff < 0. ? -diff : diff) < MIN_TIMEJUMP))	3714	if (ecb_expect_true ((diff < 0. ? -diff : diff) < MIN_TIMEJUMP))
3244	return; /* all is well */	3715	return; /* all is well */
3245		3716
3246	ev_rt_now = ev_time ();	3717	ev_rt_now = ev_time ();
3247	mn_now = get_clock ();	3718	mn_now = get_clock ();
3248	now_floor = mn_now;	3719	now_floor = mn_now;
…		…
3257	else	3728	else
3258	#endif	3729	#endif
3259	{	3730	{
3260	ev_rt_now = ev_time ();	3731	ev_rt_now = ev_time ();
3261		3732
3262	if (expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + MIN_TIMEJUMP))	3733	if (ecb_expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + MIN_TIMEJUMP))
3263	{	3734	{
3264	/* adjust timers. this is easy, as the offset is the same for all of them */	3735	/* adjust timers. this is easy, as the offset is the same for all of them */
3265	timers_reschedule (EV_A_ ev_rt_now - mn_now);	3736	timers_reschedule (EV_A_ ev_rt_now - mn_now);
3266	#if EV_PERIODIC_ENABLE	3737	#if EV_PERIODIC_ENABLE
3267	periodics_reschedule (EV_A);	3738	periodics_reschedule (EV_A);
…		…
3290	#if EV_VERIFY >= 2	3761	#if EV_VERIFY >= 2
3291	ev_verify (EV_A);	3762	ev_verify (EV_A);
3292	#endif	3763	#endif
3293		3764
3294	#ifndef _WIN32	3765	#ifndef _WIN32
3295	if (expect_false (curpid)) /* penalise the forking check even more */	3766	if (ecb_expect_false (curpid)) /* penalise the forking check even more */
3296	if (expect_false (getpid () != curpid))	3767	if (ecb_expect_false (getpid () != curpid))
3297	{	3768	{
3298	curpid = getpid ();	3769	curpid = getpid ();
3299	postfork = 1;	3770	postfork = 1;
3300	}	3771	}
3301	#endif	3772	#endif
3302		3773
3303	#if EV_FORK_ENABLE	3774	#if EV_FORK_ENABLE
3304	/* we might have forked, so queue fork handlers */	3775	/* we might have forked, so queue fork handlers */
3305	if (expect_false (postfork))	3776	if (ecb_expect_false (postfork))
3306	if (forkcnt)	3777	if (forkcnt)
3307	{	3778	{
3308	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);	3779	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);
3309	EV_INVOKE_PENDING;	3780	EV_INVOKE_PENDING;
3310	}	3781	}
3311	#endif	3782	#endif
3312		3783
3313	#if EV_PREPARE_ENABLE	3784	#if EV_PREPARE_ENABLE
3314	/* queue prepare watchers (and execute them) */	3785	/* queue prepare watchers (and execute them) */
3315	if (expect_false (preparecnt))	3786	if (ecb_expect_false (preparecnt))
3316	{	3787	{
3317	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);	3788	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);
3318	EV_INVOKE_PENDING;	3789	EV_INVOKE_PENDING;
3319	}	3790	}
3320	#endif	3791	#endif
3321		3792
3322	if (expect_false (loop_done))	3793	if (ecb_expect_false (loop_done))
3323	break;	3794	break;
3324		3795
3325	/* we might have forked, so reify kernel state if necessary */	3796	/* we might have forked, so reify kernel state if necessary */
3326	if (expect_false (postfork))	3797	if (ecb_expect_false (postfork))
3327	loop_fork (EV_A);	3798	loop_fork (EV_A);
3328		3799
3329	/* update fd-related kernel structures */	3800	/* update fd-related kernel structures */
3330	fd_reify (EV_A);	3801	fd_reify (EV_A);
3331		3802
…		…
3343	/* from now on, we want a pipe-wake-up */	3814	/* from now on, we want a pipe-wake-up */
3344	pipe_write_wanted = 1;	3815	pipe_write_wanted = 1;
3345		3816
3346	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */	3817	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */
3347		3818
3348	if (expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))	3819	if (ecb_expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))
3349	{	3820	{
3350	waittime = MAX_BLOCKTIME;	3821	waittime = MAX_BLOCKTIME;
3351		3822
3352	if (timercnt)	3823	if (timercnt)
3353	{	3824	{
…		…
3362	if (waittime > to) waittime = to;	3833	if (waittime > to) waittime = to;
3363	}	3834	}
3364	#endif	3835	#endif
3365		3836
3366	/* don't let timeouts decrease the waittime below timeout_blocktime */	3837	/* don't let timeouts decrease the waittime below timeout_blocktime */
3367	if (expect_false (waittime < timeout_blocktime))	3838	if (ecb_expect_false (waittime < timeout_blocktime))
3368	waittime = timeout_blocktime;	3839	waittime = timeout_blocktime;
3369		3840
3370	/* at this point, we NEED to wait, so we have to ensure */	3841	/* at this point, we NEED to wait, so we have to ensure */
3371	/* to pass a minimum nonzero value to the backend */	3842	/* to pass a minimum nonzero value to the backend */
3372	if (expect_false (waittime < backend_mintime))	3843	if (ecb_expect_false (waittime < backend_mintime))
3373	waittime = backend_mintime;	3844	waittime = backend_mintime;
3374		3845
3375	/* extra check because io_blocktime is commonly 0 */	3846	/* extra check because io_blocktime is commonly 0 */
3376	if (expect_false (io_blocktime))	3847	if (ecb_expect_false (io_blocktime))
3377	{	3848	{
3378	sleeptime = io_blocktime - (mn_now - prev_mn_now);	3849	sleeptime = io_blocktime - (mn_now - prev_mn_now);
3379		3850
3380	if (sleeptime > waittime - backend_mintime)	3851	if (sleeptime > waittime - backend_mintime)
3381	sleeptime = waittime - backend_mintime;	3852	sleeptime = waittime - backend_mintime;
3382		3853
3383	if (expect_true (sleeptime > 0.))	3854	if (ecb_expect_true (sleeptime > 0.))
3384	{	3855	{
3385	ev_sleep (sleeptime);	3856	ev_sleep (sleeptime);
3386	waittime -= sleeptime;	3857	waittime -= sleeptime;
3387	}	3858	}
3388	}	3859	}
…		…
3402	{	3873	{
3403	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));	3874	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));
3404	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);	3875	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);
3405	}	3876	}
3406		3877
3407
3408	/* update ev_rt_now, do magic */	3878	/* update ev_rt_now, do magic */
3409	time_update (EV_A_ waittime + sleeptime);	3879	time_update (EV_A_ waittime + sleeptime);
3410	}	3880	}
3411		3881
3412	/* queue pending timers and reschedule them */	3882	/* queue pending timers and reschedule them */
…		…
3420	idle_reify (EV_A);	3890	idle_reify (EV_A);
3421	#endif	3891	#endif
3422		3892
3423	#if EV_CHECK_ENABLE	3893	#if EV_CHECK_ENABLE
3424	/* queue check watchers, to be executed first */	3894	/* queue check watchers, to be executed first */
3425	if (expect_false (checkcnt))	3895	if (ecb_expect_false (checkcnt))
3426	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);	3896	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);
3427	#endif	3897	#endif
3428		3898
3429	EV_INVOKE_PENDING;	3899	EV_INVOKE_PENDING;
3430	}	3900	}
3431	while (expect_true (	3901	while (ecb_expect_true (
3432	activecnt	3902	activecnt
3433	&& !loop_done	3903	&& !loop_done
3434	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))	3904	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))
3435	));	3905	));
3436		3906
…		…
3443		3913
3444	return activecnt;	3914	return activecnt;
3445	}	3915	}
3446		3916
3447	void	3917	void
3448	ev_break (EV_P_ int how) EV_THROW	3918	ev_break (EV_P_ int how) EV_NOEXCEPT
3449	{	3919	{
3450	loop_done = how;	3920	loop_done = how;
3451	}	3921	}
3452		3922
3453	void	3923	void
3454	ev_ref (EV_P) EV_THROW	3924	ev_ref (EV_P) EV_NOEXCEPT
3455	{	3925	{
3456	++activecnt;	3926	++activecnt;
3457	}	3927	}
3458		3928
3459	void	3929	void
3460	ev_unref (EV_P) EV_THROW	3930	ev_unref (EV_P) EV_NOEXCEPT
3461	{	3931	{
3462	--activecnt;	3932	--activecnt;
3463	}	3933	}
3464		3934
3465	void	3935	void
3466	ev_now_update (EV_P) EV_THROW	3936	ev_now_update (EV_P) EV_NOEXCEPT
3467	{	3937	{
3468	time_update (EV_A_ 1e100);	3938	time_update (EV_A_ 1e100);
3469	}	3939	}
3470		3940
3471	void	3941	void
3472	ev_suspend (EV_P) EV_THROW	3942	ev_suspend (EV_P) EV_NOEXCEPT
3473	{	3943	{
3474	ev_now_update (EV_A);	3944	ev_now_update (EV_A);
3475	}	3945	}
3476		3946
3477	void	3947	void
3478	ev_resume (EV_P) EV_THROW	3948	ev_resume (EV_P) EV_NOEXCEPT
3479	{	3949	{
3480	ev_tstamp mn_prev = mn_now;	3950	ev_tstamp mn_prev = mn_now;
3481		3951
3482	ev_now_update (EV_A);	3952	ev_now_update (EV_A);
3483	timers_reschedule (EV_A_ mn_now - mn_prev);	3953	timers_reschedule (EV_A_ mn_now - mn_prev);
…		…
3500	inline_size void	3970	inline_size void
3501	wlist_del (WL *head, WL elem)	3971	wlist_del (WL *head, WL elem)
3502	{	3972	{
3503	while (*head)	3973	while (*head)
3504	{	3974	{
3505	if (expect_true (*head == elem))	3975	if (ecb_expect_true (*head == elem))
3506	{	3976	{
3507	*head = elem->next;	3977	*head = elem->next;
3508	break;	3978	break;
3509	}	3979	}
3510		3980
…		…
3522	w->pending = 0;	3992	w->pending = 0;
3523	}	3993	}
3524	}	3994	}
3525		3995
3526	int	3996	int
3527	ev_clear_pending (EV_P_ void *w) EV_THROW	3997	ev_clear_pending (EV_P_ void *w) EV_NOEXCEPT
3528	{	3998	{
3529	W w_ = (W)w;	3999	W w_ = (W)w;
3530	int pending = w_->pending;	4000	int pending = w_->pending;
3531		4001
3532	if (expect_true (pending))	4002	if (ecb_expect_true (pending))
3533	{	4003	{
3534	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;	4004	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;
3535	p->w = (W)&pending_w;	4005	p->w = (W)&pending_w;
3536	w_->pending = 0;	4006	w_->pending = 0;
3537	return p->events;	4007	return p->events;
…		…
3564	w->active = 0;	4034	w->active = 0;
3565	}	4035	}
3566		4036
3567	/*****************************************************************************/	4037	/*****************************************************************************/
3568		4038
3569	void noinline	4039	ecb_noinline
		4040	void
3570	ev_io_start (EV_P_ ev_io *w) EV_THROW	4041	ev_io_start (EV_P_ ev_io *w) EV_NOEXCEPT
3571	{	4042	{
3572	int fd = w->fd;	4043	int fd = w->fd;
3573		4044
3574	if (expect_false (ev_is_active (w)))	4045	if (ecb_expect_false (ev_is_active (w)))
3575	return;	4046	return;
3576		4047
3577	assert (("libev: ev_io_start called with negative fd", fd >= 0));	4048	assert (("libev: ev_io_start called with negative fd", fd >= 0));
3578	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));	4049	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));
3579		4050
		4051	#if EV_VERIFY >= 2
		4052	assert (("libev: ev_io_start called on watcher with invalid fd", fd_valid (fd)));
		4053	#endif
3580	EV_FREQUENT_CHECK;	4054	EV_FREQUENT_CHECK;
3581		4055
3582	ev_start (EV_A_ (W)w, 1);	4056	ev_start (EV_A_ (W)w, 1);
3583	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_init_zero);	4057	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_needsize_zerofill);
3584	wlist_add (&anfds[fd].head, (WL)w);	4058	wlist_add (&anfds[fd].head, (WL)w);
3585		4059
3586	/* common bug, apparently */	4060	/* common bug, apparently */
3587	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));	4061	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));
3588		4062
…		…
3590	w->events &= ~EV__IOFDSET;	4064	w->events &= ~EV__IOFDSET;
3591		4065
3592	EV_FREQUENT_CHECK;	4066	EV_FREQUENT_CHECK;
3593	}	4067	}
3594		4068
3595	void noinline	4069	ecb_noinline
		4070	void
3596	ev_io_stop (EV_P_ ev_io *w) EV_THROW	4071	ev_io_stop (EV_P_ ev_io *w) EV_NOEXCEPT
3597	{	4072	{
3598	clear_pending (EV_A_ (W)w);	4073	clear_pending (EV_A_ (W)w);
3599	if (expect_false (!ev_is_active (w)))	4074	if (ecb_expect_false (!ev_is_active (w)))
3600	return;	4075	return;
3601		4076
3602	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));	4077	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));
3603		4078
		4079	#if EV_VERIFY >= 2
		4080	assert (("libev: ev_io_stop called on watcher with invalid fd", fd_valid (w->fd)));
		4081	#endif
3604	EV_FREQUENT_CHECK;	4082	EV_FREQUENT_CHECK;
3605		4083
3606	wlist_del (&anfds[w->fd].head, (WL)w);	4084	wlist_del (&anfds[w->fd].head, (WL)w);
3607	ev_stop (EV_A_ (W)w);	4085	ev_stop (EV_A_ (W)w);
3608		4086
3609	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);	4087	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);
3610		4088
3611	EV_FREQUENT_CHECK;	4089	EV_FREQUENT_CHECK;
3612	}	4090	}
3613		4091
3614	void noinline	4092	ecb_noinline
		4093	void
3615	ev_timer_start (EV_P_ ev_timer *w) EV_THROW	4094	ev_timer_start (EV_P_ ev_timer *w) EV_NOEXCEPT
3616	{	4095	{
3617	if (expect_false (ev_is_active (w)))	4096	if (ecb_expect_false (ev_is_active (w)))
3618	return;	4097	return;
3619		4098
3620	ev_at (w) += mn_now;	4099	ev_at (w) += mn_now;
3621		4100
3622	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));	4101	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));
3623		4102
3624	EV_FREQUENT_CHECK;	4103	EV_FREQUENT_CHECK;
3625		4104
3626	++timercnt;	4105	++timercnt;
3627	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);	4106	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);
3628	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, EMPTY2);	4107	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, array_needsize_noinit);
3629	ANHE_w (timers [ev_active (w)]) = (WT)w;	4108	ANHE_w (timers [ev_active (w)]) = (WT)w;
3630	ANHE_at_cache (timers [ev_active (w)]);	4109	ANHE_at_cache (timers [ev_active (w)]);
3631	upheap (timers, ev_active (w));	4110	upheap (timers, ev_active (w));
3632		4111
3633	EV_FREQUENT_CHECK;	4112	EV_FREQUENT_CHECK;
3634		4113
3635	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/	4114	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/
3636	}	4115	}
3637		4116
3638	void noinline	4117	ecb_noinline
		4118	void
3639	ev_timer_stop (EV_P_ ev_timer *w) EV_THROW	4119	ev_timer_stop (EV_P_ ev_timer *w) EV_NOEXCEPT
3640	{	4120	{
3641	clear_pending (EV_A_ (W)w);	4121	clear_pending (EV_A_ (W)w);
3642	if (expect_false (!ev_is_active (w)))	4122	if (ecb_expect_false (!ev_is_active (w)))
3643	return;	4123	return;
3644		4124
3645	EV_FREQUENT_CHECK;	4125	EV_FREQUENT_CHECK;
3646		4126
3647	{	4127	{
…		…
3649		4129
3650	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));	4130	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));
3651		4131
3652	--timercnt;	4132	--timercnt;
3653		4133
3654	if (expect_true (active < timercnt + HEAP0))	4134	if (ecb_expect_true (active < timercnt + HEAP0))
3655	{	4135	{
3656	timers [active] = timers [timercnt + HEAP0];	4136	timers [active] = timers [timercnt + HEAP0];
3657	adjustheap (timers, timercnt, active);	4137	adjustheap (timers, timercnt, active);
3658	}	4138	}
3659	}	4139	}
…		…
3663	ev_stop (EV_A_ (W)w);	4143	ev_stop (EV_A_ (W)w);
3664		4144
3665	EV_FREQUENT_CHECK;	4145	EV_FREQUENT_CHECK;
3666	}	4146	}
3667		4147
3668	void noinline	4148	ecb_noinline
		4149	void
3669	ev_timer_again (EV_P_ ev_timer *w) EV_THROW	4150	ev_timer_again (EV_P_ ev_timer *w) EV_NOEXCEPT
3670	{	4151	{
3671	EV_FREQUENT_CHECK;	4152	EV_FREQUENT_CHECK;
3672		4153
3673	clear_pending (EV_A_ (W)w);	4154	clear_pending (EV_A_ (W)w);
3674		4155
…		…
3691		4172
3692	EV_FREQUENT_CHECK;	4173	EV_FREQUENT_CHECK;
3693	}	4174	}
3694		4175
3695	ev_tstamp	4176	ev_tstamp
3696	ev_timer_remaining (EV_P_ ev_timer *w) EV_THROW	4177	ev_timer_remaining (EV_P_ ev_timer *w) EV_NOEXCEPT
3697	{	4178	{
3698	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);	4179	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);
3699	}	4180	}
3700		4181
3701	#if EV_PERIODIC_ENABLE	4182	#if EV_PERIODIC_ENABLE
3702	void noinline	4183	ecb_noinline
		4184	void
3703	ev_periodic_start (EV_P_ ev_periodic *w) EV_THROW	4185	ev_periodic_start (EV_P_ ev_periodic *w) EV_NOEXCEPT
3704	{	4186	{
3705	if (expect_false (ev_is_active (w)))	4187	if (ecb_expect_false (ev_is_active (w)))
3706	return;	4188	return;
3707		4189
3708	if (w->reschedule_cb)	4190	if (w->reschedule_cb)
3709	ev_at (w) = w->reschedule_cb (w, ev_rt_now);	4191	ev_at (w) = w->reschedule_cb (w, ev_rt_now);
3710	else if (w->interval)	4192	else if (w->interval)
…		…
3717		4199
3718	EV_FREQUENT_CHECK;	4200	EV_FREQUENT_CHECK;
3719		4201
3720	++periodiccnt;	4202	++periodiccnt;
3721	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);	4203	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);
3722	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, EMPTY2);	4204	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, array_needsize_noinit);
3723	ANHE_w (periodics [ev_active (w)]) = (WT)w;	4205	ANHE_w (periodics [ev_active (w)]) = (WT)w;
3724	ANHE_at_cache (periodics [ev_active (w)]);	4206	ANHE_at_cache (periodics [ev_active (w)]);
3725	upheap (periodics, ev_active (w));	4207	upheap (periodics, ev_active (w));
3726		4208
3727	EV_FREQUENT_CHECK;	4209	EV_FREQUENT_CHECK;
3728		4210
3729	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/	4211	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/
3730	}	4212	}
3731		4213
3732	void noinline	4214	ecb_noinline
		4215	void
3733	ev_periodic_stop (EV_P_ ev_periodic *w) EV_THROW	4216	ev_periodic_stop (EV_P_ ev_periodic *w) EV_NOEXCEPT
3734	{	4217	{
3735	clear_pending (EV_A_ (W)w);	4218	clear_pending (EV_A_ (W)w);
3736	if (expect_false (!ev_is_active (w)))	4219	if (ecb_expect_false (!ev_is_active (w)))
3737	return;	4220	return;
3738		4221
3739	EV_FREQUENT_CHECK;	4222	EV_FREQUENT_CHECK;
3740		4223
3741	{	4224	{
…		…
3743		4226
3744	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));	4227	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));
3745		4228
3746	--periodiccnt;	4229	--periodiccnt;
3747		4230
3748	if (expect_true (active < periodiccnt + HEAP0))	4231	if (ecb_expect_true (active < periodiccnt + HEAP0))
3749	{	4232	{
3750	periodics [active] = periodics [periodiccnt + HEAP0];	4233	periodics [active] = periodics [periodiccnt + HEAP0];
3751	adjustheap (periodics, periodiccnt, active);	4234	adjustheap (periodics, periodiccnt, active);
3752	}	4235	}
3753	}	4236	}
…		…
3755	ev_stop (EV_A_ (W)w);	4238	ev_stop (EV_A_ (W)w);
3756		4239
3757	EV_FREQUENT_CHECK;	4240	EV_FREQUENT_CHECK;
3758	}	4241	}
3759		4242
3760	void noinline	4243	ecb_noinline
		4244	void
3761	ev_periodic_again (EV_P_ ev_periodic *w) EV_THROW	4245	ev_periodic_again (EV_P_ ev_periodic *w) EV_NOEXCEPT
3762	{	4246	{
3763	/* TODO: use adjustheap and recalculation */	4247	/* TODO: use adjustheap and recalculation */
3764	ev_periodic_stop (EV_A_ w);	4248	ev_periodic_stop (EV_A_ w);
3765	ev_periodic_start (EV_A_ w);	4249	ev_periodic_start (EV_A_ w);
3766	}	4250	}
…		…
3770	# define SA_RESTART 0	4254	# define SA_RESTART 0
3771	#endif	4255	#endif
3772		4256
3773	#if EV_SIGNAL_ENABLE	4257	#if EV_SIGNAL_ENABLE
3774		4258
3775	void noinline	4259	ecb_noinline
		4260	void
3776	ev_signal_start (EV_P_ ev_signal *w) EV_THROW	4261	ev_signal_start (EV_P_ ev_signal *w) EV_NOEXCEPT
3777	{	4262	{
3778	if (expect_false (ev_is_active (w)))	4263	if (ecb_expect_false (ev_is_active (w)))
3779	return;	4264	return;
3780		4265
3781	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));	4266	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));
3782		4267
3783	#if EV_MULTIPLICITY	4268	#if EV_MULTIPLICITY
…		…
3852	}	4337	}
3853		4338
3854	EV_FREQUENT_CHECK;	4339	EV_FREQUENT_CHECK;
3855	}	4340	}
3856		4341
3857	void noinline	4342	ecb_noinline
		4343	void
3858	ev_signal_stop (EV_P_ ev_signal *w) EV_THROW	4344	ev_signal_stop (EV_P_ ev_signal *w) EV_NOEXCEPT
3859	{	4345	{
3860	clear_pending (EV_A_ (W)w);	4346	clear_pending (EV_A_ (W)w);
3861	if (expect_false (!ev_is_active (w)))	4347	if (ecb_expect_false (!ev_is_active (w)))
3862	return;	4348	return;
3863		4349
3864	EV_FREQUENT_CHECK;	4350	EV_FREQUENT_CHECK;
3865		4351
3866	wlist_del (&signals [w->signum - 1].head, (WL)w);	4352	wlist_del (&signals [w->signum - 1].head, (WL)w);
…		…
3894	#endif	4380	#endif
3895		4381
3896	#if EV_CHILD_ENABLE	4382	#if EV_CHILD_ENABLE
3897		4383
3898	void	4384	void
3899	ev_child_start (EV_P_ ev_child *w) EV_THROW	4385	ev_child_start (EV_P_ ev_child *w) EV_NOEXCEPT
3900	{	4386	{
3901	#if EV_MULTIPLICITY	4387	#if EV_MULTIPLICITY
3902	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));	4388	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));
3903	#endif	4389	#endif
3904	if (expect_false (ev_is_active (w)))	4390	if (ecb_expect_false (ev_is_active (w)))
3905	return;	4391	return;
3906		4392
3907	EV_FREQUENT_CHECK;	4393	EV_FREQUENT_CHECK;
3908		4394
3909	ev_start (EV_A_ (W)w, 1);	4395	ev_start (EV_A_ (W)w, 1);
…		…
3911		4397
3912	EV_FREQUENT_CHECK;	4398	EV_FREQUENT_CHECK;
3913	}	4399	}
3914		4400
3915	void	4401	void
3916	ev_child_stop (EV_P_ ev_child *w) EV_THROW	4402	ev_child_stop (EV_P_ ev_child *w) EV_NOEXCEPT
3917	{	4403	{
3918	clear_pending (EV_A_ (W)w);	4404	clear_pending (EV_A_ (W)w);
3919	if (expect_false (!ev_is_active (w)))	4405	if (ecb_expect_false (!ev_is_active (w)))
3920	return;	4406	return;
3921		4407
3922	EV_FREQUENT_CHECK;	4408	EV_FREQUENT_CHECK;
3923		4409
3924	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);	4410	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);
…		…
3938		4424
3939	#define DEF_STAT_INTERVAL 5.0074891	4425	#define DEF_STAT_INTERVAL 5.0074891
3940	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */	4426	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */
3941	#define MIN_STAT_INTERVAL 0.1074891	4427	#define MIN_STAT_INTERVAL 0.1074891
3942		4428
3943	static void noinline stat_timer_cb (EV_P_ ev_timer *w_, int revents);	4429	ecb_noinline static void stat_timer_cb (EV_P_ ev_timer *w_, int revents);
3944		4430
3945	#if EV_USE_INOTIFY	4431	#if EV_USE_INOTIFY
3946		4432
3947	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */	4433	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */
3948	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)	4434	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)
3949		4435
3950	static void noinline	4436	ecb_noinline
		4437	static void
3951	infy_add (EV_P_ ev_stat *w)	4438	infy_add (EV_P_ ev_stat *w)
3952	{	4439	{
3953	w->wd = inotify_add_watch (fs_fd, w->path,	4440	w->wd = inotify_add_watch (fs_fd, w->path,
3954	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY	4441	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY
3955	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO	4442	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO
…		…
4019	if (ev_is_active (&w->timer)) ev_ref (EV_A);	4506	if (ev_is_active (&w->timer)) ev_ref (EV_A);
4020	ev_timer_again (EV_A_ &w->timer);	4507	ev_timer_again (EV_A_ &w->timer);
4021	if (ev_is_active (&w->timer)) ev_unref (EV_A);	4508	if (ev_is_active (&w->timer)) ev_unref (EV_A);
4022	}	4509	}
4023		4510
4024	static void noinline	4511	ecb_noinline
		4512	static void
4025	infy_del (EV_P_ ev_stat *w)	4513	infy_del (EV_P_ ev_stat *w)
4026	{	4514	{
4027	int slot;	4515	int slot;
4028	int wd = w->wd;	4516	int wd = w->wd;
4029		4517
…		…
4036		4524
4037	/* remove this watcher, if others are watching it, they will rearm */	4525	/* remove this watcher, if others are watching it, they will rearm */
4038	inotify_rm_watch (fs_fd, wd);	4526	inotify_rm_watch (fs_fd, wd);
4039	}	4527	}
4040		4528
4041	static void noinline	4529	ecb_noinline
		4530	static void
4042	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)	4531	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)
4043	{	4532	{
4044	if (slot < 0)	4533	if (slot < 0)
4045	/* overflow, need to check for all hash slots */	4534	/* overflow, need to check for all hash slots */
4046	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)	4535	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)
…		…
4082	infy_wd (EV_A_ ev->wd, ev->wd, ev);	4571	infy_wd (EV_A_ ev->wd, ev->wd, ev);
4083	ofs += sizeof (struct inotify_event) + ev->len;	4572	ofs += sizeof (struct inotify_event) + ev->len;
4084	}	4573	}
4085	}	4574	}
4086		4575
4087	inline_size void ecb_cold	4576	inline_size ecb_cold
		4577	void
4088	ev_check_2625 (EV_P)	4578	ev_check_2625 (EV_P)
4089	{	4579	{
4090	/* kernels < 2.6.25 are borked	4580	/* kernels < 2.6.25 are borked
4091	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html	4581	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html
4092	*/	4582	*/
…		…
4182	#else	4672	#else
4183	# define EV_LSTAT(p,b) lstat (p, b)	4673	# define EV_LSTAT(p,b) lstat (p, b)
4184	#endif	4674	#endif
4185		4675
4186	void	4676	void
4187	ev_stat_stat (EV_P_ ev_stat *w) EV_THROW	4677	ev_stat_stat (EV_P_ ev_stat *w) EV_NOEXCEPT
4188	{	4678	{
4189	if (lstat (w->path, &w->attr) < 0)	4679	if (lstat (w->path, &w->attr) < 0)
4190	w->attr.st_nlink = 0;	4680	w->attr.st_nlink = 0;
4191	else if (!w->attr.st_nlink)	4681	else if (!w->attr.st_nlink)
4192	w->attr.st_nlink = 1;	4682	w->attr.st_nlink = 1;
4193	}	4683	}
4194		4684
4195	static void noinline	4685	ecb_noinline
		4686	static void
4196	stat_timer_cb (EV_P_ ev_timer *w_, int revents)	4687	stat_timer_cb (EV_P_ ev_timer *w_, int revents)
4197	{	4688	{
4198	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));	4689	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));
4199		4690
4200	ev_statdata prev = w->attr;	4691	ev_statdata prev = w->attr;
…		…
4231	ev_feed_event (EV_A_ w, EV_STAT);	4722	ev_feed_event (EV_A_ w, EV_STAT);
4232	}	4723	}
4233	}	4724	}
4234		4725
4235	void	4726	void
4236	ev_stat_start (EV_P_ ev_stat *w) EV_THROW	4727	ev_stat_start (EV_P_ ev_stat *w) EV_NOEXCEPT
4237	{	4728	{
4238	if (expect_false (ev_is_active (w)))	4729	if (ecb_expect_false (ev_is_active (w)))
4239	return;	4730	return;
4240		4731
4241	ev_stat_stat (EV_A_ w);	4732	ev_stat_stat (EV_A_ w);
4242		4733
4243	if (w->interval < MIN_STAT_INTERVAL && w->interval)	4734	if (w->interval < MIN_STAT_INTERVAL && w->interval)
…		…
4262		4753
4263	EV_FREQUENT_CHECK;	4754	EV_FREQUENT_CHECK;
4264	}	4755	}
4265		4756
4266	void	4757	void
4267	ev_stat_stop (EV_P_ ev_stat *w) EV_THROW	4758	ev_stat_stop (EV_P_ ev_stat *w) EV_NOEXCEPT
4268	{	4759	{
4269	clear_pending (EV_A_ (W)w);	4760	clear_pending (EV_A_ (W)w);
4270	if (expect_false (!ev_is_active (w)))	4761	if (ecb_expect_false (!ev_is_active (w)))
4271	return;	4762	return;
4272		4763
4273	EV_FREQUENT_CHECK;	4764	EV_FREQUENT_CHECK;
4274		4765
4275	#if EV_USE_INOTIFY	4766	#if EV_USE_INOTIFY
…		…
4288	}	4779	}
4289	#endif	4780	#endif
4290		4781
4291	#if EV_IDLE_ENABLE	4782	#if EV_IDLE_ENABLE
4292	void	4783	void
4293	ev_idle_start (EV_P_ ev_idle *w) EV_THROW	4784	ev_idle_start (EV_P_ ev_idle *w) EV_NOEXCEPT
4294	{	4785	{
4295	if (expect_false (ev_is_active (w)))	4786	if (ecb_expect_false (ev_is_active (w)))
4296	return;	4787	return;
4297		4788
4298	pri_adjust (EV_A_ (W)w);	4789	pri_adjust (EV_A_ (W)w);
4299		4790
4300	EV_FREQUENT_CHECK;	4791	EV_FREQUENT_CHECK;
…		…
4303	int active = ++idlecnt [ABSPRI (w)];	4794	int active = ++idlecnt [ABSPRI (w)];
4304		4795
4305	++idleall;	4796	++idleall;
4306	ev_start (EV_A_ (W)w, active);	4797	ev_start (EV_A_ (W)w, active);
4307		4798
4308	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, EMPTY2);	4799	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, array_needsize_noinit);
4309	idles [ABSPRI (w)][active - 1] = w;	4800	idles [ABSPRI (w)][active - 1] = w;
4310	}	4801	}
4311		4802
4312	EV_FREQUENT_CHECK;	4803	EV_FREQUENT_CHECK;
4313	}	4804	}
4314		4805
4315	void	4806	void
4316	ev_idle_stop (EV_P_ ev_idle *w) EV_THROW	4807	ev_idle_stop (EV_P_ ev_idle *w) EV_NOEXCEPT
4317	{	4808	{
4318	clear_pending (EV_A_ (W)w);	4809	clear_pending (EV_A_ (W)w);
4319	if (expect_false (!ev_is_active (w)))	4810	if (ecb_expect_false (!ev_is_active (w)))
4320	return;	4811	return;
4321		4812
4322	EV_FREQUENT_CHECK;	4813	EV_FREQUENT_CHECK;
4323		4814
4324	{	4815	{
…		…
4335	}	4826	}
4336	#endif	4827	#endif
4337		4828
4338	#if EV_PREPARE_ENABLE	4829	#if EV_PREPARE_ENABLE
4339	void	4830	void
4340	ev_prepare_start (EV_P_ ev_prepare *w) EV_THROW	4831	ev_prepare_start (EV_P_ ev_prepare *w) EV_NOEXCEPT
4341	{	4832	{
4342	if (expect_false (ev_is_active (w)))	4833	if (ecb_expect_false (ev_is_active (w)))
4343	return;	4834	return;
4344		4835
4345	EV_FREQUENT_CHECK;	4836	EV_FREQUENT_CHECK;
4346		4837
4347	ev_start (EV_A_ (W)w, ++preparecnt);	4838	ev_start (EV_A_ (W)w, ++preparecnt);
4348	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, EMPTY2);	4839	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, array_needsize_noinit);
4349	prepares [preparecnt - 1] = w;	4840	prepares [preparecnt - 1] = w;
4350		4841
4351	EV_FREQUENT_CHECK;	4842	EV_FREQUENT_CHECK;
4352	}	4843	}
4353		4844
4354	void	4845	void
4355	ev_prepare_stop (EV_P_ ev_prepare *w) EV_THROW	4846	ev_prepare_stop (EV_P_ ev_prepare *w) EV_NOEXCEPT
4356	{	4847	{
4357	clear_pending (EV_A_ (W)w);	4848	clear_pending (EV_A_ (W)w);
4358	if (expect_false (!ev_is_active (w)))	4849	if (ecb_expect_false (!ev_is_active (w)))
4359	return;	4850	return;
4360		4851
4361	EV_FREQUENT_CHECK;	4852	EV_FREQUENT_CHECK;
4362		4853
4363	{	4854	{
…		…
4373	}	4864	}
4374	#endif	4865	#endif
4375		4866
4376	#if EV_CHECK_ENABLE	4867	#if EV_CHECK_ENABLE
4377	void	4868	void
4378	ev_check_start (EV_P_ ev_check *w) EV_THROW	4869	ev_check_start (EV_P_ ev_check *w) EV_NOEXCEPT
4379	{	4870	{
4380	if (expect_false (ev_is_active (w)))	4871	if (ecb_expect_false (ev_is_active (w)))
4381	return;	4872	return;
4382		4873
4383	EV_FREQUENT_CHECK;	4874	EV_FREQUENT_CHECK;
4384		4875
4385	ev_start (EV_A_ (W)w, ++checkcnt);	4876	ev_start (EV_A_ (W)w, ++checkcnt);
4386	array_needsize (ev_check *, checks, checkmax, checkcnt, EMPTY2);	4877	array_needsize (ev_check *, checks, checkmax, checkcnt, array_needsize_noinit);
4387	checks [checkcnt - 1] = w;	4878	checks [checkcnt - 1] = w;
4388		4879
4389	EV_FREQUENT_CHECK;	4880	EV_FREQUENT_CHECK;
4390	}	4881	}
4391		4882
4392	void	4883	void
4393	ev_check_stop (EV_P_ ev_check *w) EV_THROW	4884	ev_check_stop (EV_P_ ev_check *w) EV_NOEXCEPT
4394	{	4885	{
4395	clear_pending (EV_A_ (W)w);	4886	clear_pending (EV_A_ (W)w);
4396	if (expect_false (!ev_is_active (w)))	4887	if (ecb_expect_false (!ev_is_active (w)))
4397	return;	4888	return;
4398		4889
4399	EV_FREQUENT_CHECK;	4890	EV_FREQUENT_CHECK;
4400		4891
4401	{	4892	{
…		…
4410	EV_FREQUENT_CHECK;	4901	EV_FREQUENT_CHECK;
4411	}	4902	}
4412	#endif	4903	#endif
4413		4904
4414	#if EV_EMBED_ENABLE	4905	#if EV_EMBED_ENABLE
4415	void noinline	4906	ecb_noinline
		4907	void
4416	ev_embed_sweep (EV_P_ ev_embed *w) EV_THROW	4908	ev_embed_sweep (EV_P_ ev_embed *w) EV_NOEXCEPT
4417	{	4909	{
4418	ev_run (w->other, EVRUN_NOWAIT);	4910	ev_run (w->other, EVRUN_NOWAIT);
4419	}	4911	}
4420		4912
4421	static void	4913	static void
…		…
4469	ev_idle_stop (EV_A_ idle);	4961	ev_idle_stop (EV_A_ idle);
4470	}	4962	}
4471	#endif	4963	#endif
4472		4964
4473	void	4965	void
4474	ev_embed_start (EV_P_ ev_embed *w) EV_THROW	4966	ev_embed_start (EV_P_ ev_embed *w) EV_NOEXCEPT
4475	{	4967	{
4476	if (expect_false (ev_is_active (w)))	4968	if (ecb_expect_false (ev_is_active (w)))
4477	return;	4969	return;
4478		4970
4479	{	4971	{
4480	EV_P = w->other;	4972	EV_P = w->other;
4481	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));	4973	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));
…		…
4500		4992
4501	EV_FREQUENT_CHECK;	4993	EV_FREQUENT_CHECK;
4502	}	4994	}
4503		4995
4504	void	4996	void
4505	ev_embed_stop (EV_P_ ev_embed *w) EV_THROW	4997	ev_embed_stop (EV_P_ ev_embed *w) EV_NOEXCEPT
4506	{	4998	{
4507	clear_pending (EV_A_ (W)w);	4999	clear_pending (EV_A_ (W)w);
4508	if (expect_false (!ev_is_active (w)))	5000	if (ecb_expect_false (!ev_is_active (w)))
4509	return;	5001	return;
4510		5002
4511	EV_FREQUENT_CHECK;	5003	EV_FREQUENT_CHECK;
4512		5004
4513	ev_io_stop (EV_A_ &w->io);	5005	ev_io_stop (EV_A_ &w->io);
…		…
4520	}	5012	}
4521	#endif	5013	#endif
4522		5014
4523	#if EV_FORK_ENABLE	5015	#if EV_FORK_ENABLE
4524	void	5016	void
4525	ev_fork_start (EV_P_ ev_fork *w) EV_THROW	5017	ev_fork_start (EV_P_ ev_fork *w) EV_NOEXCEPT
4526	{	5018	{
4527	if (expect_false (ev_is_active (w)))	5019	if (ecb_expect_false (ev_is_active (w)))
4528	return;	5020	return;
4529		5021
4530	EV_FREQUENT_CHECK;	5022	EV_FREQUENT_CHECK;
4531		5023
4532	ev_start (EV_A_ (W)w, ++forkcnt);	5024	ev_start (EV_A_ (W)w, ++forkcnt);
4533	array_needsize (ev_fork *, forks, forkmax, forkcnt, EMPTY2);	5025	array_needsize (ev_fork *, forks, forkmax, forkcnt, array_needsize_noinit);
4534	forks [forkcnt - 1] = w;	5026	forks [forkcnt - 1] = w;
4535		5027
4536	EV_FREQUENT_CHECK;	5028	EV_FREQUENT_CHECK;
4537	}	5029	}
4538		5030
4539	void	5031	void
4540	ev_fork_stop (EV_P_ ev_fork *w) EV_THROW	5032	ev_fork_stop (EV_P_ ev_fork *w) EV_NOEXCEPT
4541	{	5033	{
4542	clear_pending (EV_A_ (W)w);	5034	clear_pending (EV_A_ (W)w);
4543	if (expect_false (!ev_is_active (w)))	5035	if (ecb_expect_false (!ev_is_active (w)))
4544	return;	5036	return;
4545		5037
4546	EV_FREQUENT_CHECK;	5038	EV_FREQUENT_CHECK;
4547		5039
4548	{	5040	{
…		…
4558	}	5050	}
4559	#endif	5051	#endif
4560		5052
4561	#if EV_CLEANUP_ENABLE	5053	#if EV_CLEANUP_ENABLE
4562	void	5054	void
4563	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_THROW	5055	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4564	{	5056	{
4565	if (expect_false (ev_is_active (w)))	5057	if (ecb_expect_false (ev_is_active (w)))
4566	return;	5058	return;
4567		5059
4568	EV_FREQUENT_CHECK;	5060	EV_FREQUENT_CHECK;
4569		5061
4570	ev_start (EV_A_ (W)w, ++cleanupcnt);	5062	ev_start (EV_A_ (W)w, ++cleanupcnt);
4571	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, EMPTY2);	5063	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, array_needsize_noinit);
4572	cleanups [cleanupcnt - 1] = w;	5064	cleanups [cleanupcnt - 1] = w;
4573		5065
4574	/* cleanup watchers should never keep a refcount on the loop */	5066	/* cleanup watchers should never keep a refcount on the loop */
4575	ev_unref (EV_A);	5067	ev_unref (EV_A);
4576	EV_FREQUENT_CHECK;	5068	EV_FREQUENT_CHECK;
4577	}	5069	}
4578		5070
4579	void	5071	void
4580	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_THROW	5072	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4581	{	5073	{
4582	clear_pending (EV_A_ (W)w);	5074	clear_pending (EV_A_ (W)w);
4583	if (expect_false (!ev_is_active (w)))	5075	if (ecb_expect_false (!ev_is_active (w)))
4584	return;	5076	return;
4585		5077
4586	EV_FREQUENT_CHECK;	5078	EV_FREQUENT_CHECK;
4587	ev_ref (EV_A);	5079	ev_ref (EV_A);
4588		5080
…		…
4599	}	5091	}
4600	#endif	5092	#endif
4601		5093
4602	#if EV_ASYNC_ENABLE	5094	#if EV_ASYNC_ENABLE
4603	void	5095	void
4604	ev_async_start (EV_P_ ev_async *w) EV_THROW	5096	ev_async_start (EV_P_ ev_async *w) EV_NOEXCEPT
4605	{	5097	{
4606	if (expect_false (ev_is_active (w)))	5098	if (ecb_expect_false (ev_is_active (w)))
4607	return;	5099	return;
4608		5100
4609	w->sent = 0;	5101	w->sent = 0;
4610		5102
4611	evpipe_init (EV_A);	5103	evpipe_init (EV_A);
4612		5104
4613	EV_FREQUENT_CHECK;	5105	EV_FREQUENT_CHECK;
4614		5106
4615	ev_start (EV_A_ (W)w, ++asynccnt);	5107	ev_start (EV_A_ (W)w, ++asynccnt);
4616	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, EMPTY2);	5108	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, array_needsize_noinit);
4617	asyncs [asynccnt - 1] = w;	5109	asyncs [asynccnt - 1] = w;
4618		5110
4619	EV_FREQUENT_CHECK;	5111	EV_FREQUENT_CHECK;
4620	}	5112	}
4621		5113
4622	void	5114	void
4623	ev_async_stop (EV_P_ ev_async *w) EV_THROW	5115	ev_async_stop (EV_P_ ev_async *w) EV_NOEXCEPT
4624	{	5116	{
4625	clear_pending (EV_A_ (W)w);	5117	clear_pending (EV_A_ (W)w);
4626	if (expect_false (!ev_is_active (w)))	5118	if (ecb_expect_false (!ev_is_active (w)))
4627	return;	5119	return;
4628		5120
4629	EV_FREQUENT_CHECK;	5121	EV_FREQUENT_CHECK;
4630		5122
4631	{	5123	{
…		…
4639		5131
4640	EV_FREQUENT_CHECK;	5132	EV_FREQUENT_CHECK;
4641	}	5133	}
4642		5134
4643	void	5135	void
4644	ev_async_send (EV_P_ ev_async *w) EV_THROW	5136	ev_async_send (EV_P_ ev_async *w) EV_NOEXCEPT
4645	{	5137	{
4646	w->sent = 1;	5138	w->sent = 1;
4647	evpipe_write (EV_A_ &async_pending);	5139	evpipe_write (EV_A_ &async_pending);
4648	}	5140	}
4649	#endif	5141	#endif
…		…
4686		5178
4687	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));	5179	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));
4688	}	5180	}
4689		5181
4690	void	5182	void
4691	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_THROW	5183	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_NOEXCEPT
4692	{	5184	{
4693	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));	5185	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));
4694
4695	if (expect_false (!once))
4696	{
4697	cb (EV_ERROR | EV_READ | EV_WRITE | EV_TIMER, arg);
4698	return;
4699	}
4700		5186
4701	once->cb = cb;	5187	once->cb = cb;
4702	once->arg = arg;	5188	once->arg = arg;
4703		5189
4704	ev_init (&once->io, once_cb_io);	5190	ev_init (&once->io, once_cb_io);
…		…
4717	}	5203	}
4718		5204
4719	/*****************************************************************************/	5205	/*****************************************************************************/
4720		5206
4721	#if EV_WALK_ENABLE	5207	#if EV_WALK_ENABLE
4722	void ecb_cold	5208	ecb_cold
		5209	void
4723	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_THROW	5210	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_NOEXCEPT
4724	{	5211	{
4725	int i, j;	5212	int i, j;
4726	ev_watcher_list *wl, *wn;	5213	ev_watcher_list *wl, *wn;
4727		5214
4728	if (types & (EV_IO | EV_EMBED))	5215	if (types & (EV_IO | EV_EMBED))

Diff Legend

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