ViewVC Help

View File | Revision Log | Show Annotations | Download File

/cvs/libev/ev.c

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

Diff Legend

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