ViewVC Help

View File | Revision Log | Show Annotations | Download File

/cvs/libev/ev.c

Comparing libev/ev.c (file contents):
Revision 1.426 by root, Sun May 6 13:42:10 2012 UTC vs.
Revision 1.498 by root, Wed Jun 26 00:01:46 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
…		…
201	# include <sys/wait.h>	220	# include <sys/wait.h>
202	# include <unistd.h>	221	# include <unistd.h>
203	#else	222	#else
204	# include <io.h>	223	# include <io.h>
205	# define WIN32_LEAN_AND_MEAN	224	# define WIN32_LEAN_AND_MEAN
		225	# include <winsock2.h>
206	# include <windows.h>	226	# include <windows.h>
207	# ifndef EV_SELECT_IS_WINSOCKET	227	# ifndef EV_SELECT_IS_WINSOCKET
208	# define EV_SELECT_IS_WINSOCKET 1	228	# define EV_SELECT_IS_WINSOCKET 1
209	# endif	229	# endif
210	# undef EV_AVOID_STDIO	230	# undef EV_AVOID_STDIO
211	#endif	231	#endif
212
213	/* OS X, in its infinite idiocy, actually HARDCODES
214	* a limit of 1024 into their select. Where people have brains,
215	* OS X engineers apparently have a vacuum. Or maybe they were
216	* ordered to have a vacuum, or they do anything for money.
217	* This might help. Or not.
218	*/
219	#define _DARWIN_UNLIMITED_SELECT 1
220		232
221	/* 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 */
222		234
223	/* try to deduce the maximum number of signals on this platform */	235	/* try to deduce the maximum number of signals on this platform */
224	#if defined EV_NSIG	236	#if defined EV_NSIG
…		…
240	#elif defined SIGARRAYSIZE	252	#elif defined SIGARRAYSIZE
241	# define EV_NSIG (SIGARRAYSIZE) /* Assume ary[SIGARRAYSIZE] */	253	# define EV_NSIG (SIGARRAYSIZE) /* Assume ary[SIGARRAYSIZE] */
242	#elif defined _sys_nsig	254	#elif defined _sys_nsig
243	# define EV_NSIG (_sys_nsig) /* Solaris 2.5 */	255	# define EV_NSIG (_sys_nsig) /* Solaris 2.5 */
244	#else	256	#else
245	# error "unable to find value for NSIG, please report"	257	# define EV_NSIG (8 * sizeof (sigset_t) + 1)
246	/* to make it compile regardless, just remove the above line, */
247	/* but consider reporting it, too! :) */
248	# define EV_NSIG 65
249	#endif	258	#endif
250		259
251	#ifndef EV_USE_FLOOR	260	#ifndef EV_USE_FLOOR
252	# define EV_USE_FLOOR 0	261	# define EV_USE_FLOOR 0
253	#endif	262	#endif
254		263
255	#ifndef EV_USE_CLOCK_SYSCALL	264	#ifndef EV_USE_CLOCK_SYSCALL
256	# if __linux && __GLIBC__ >= 2	265	# if __linux && __GLIBC__ == 2 && __GLIBC_MINOR__ < 17
257	# define EV_USE_CLOCK_SYSCALL EV_FEATURE_OS	266	# define EV_USE_CLOCK_SYSCALL EV_FEATURE_OS
258	# else	267	# else
259	# 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
260	# endif	278	# endif
261	#endif	279	#endif
262		280
263	#ifndef EV_USE_MONOTONIC	281	#ifndef EV_USE_MONOTONIC
264	# if defined _POSIX_MONOTONIC_CLOCK && _POSIX_MONOTONIC_CLOCK >= 0	282	# if defined _POSIX_MONOTONIC_CLOCK && _POSIX_MONOTONIC_CLOCK >= 0
…		…
306		324
307	#ifndef EV_USE_PORT	325	#ifndef EV_USE_PORT
308	# define EV_USE_PORT 0	326	# define EV_USE_PORT 0
309	#endif	327	#endif
310		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
311	#ifndef EV_USE_INOTIFY	337	#ifndef EV_USE_INOTIFY
312	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))	338	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))
313	# define EV_USE_INOTIFY EV_FEATURE_OS	339	# define EV_USE_INOTIFY EV_FEATURE_OS
314	# else	340	# else
315	# define EV_USE_INOTIFY 0	341	# define EV_USE_INOTIFY 0
…		…
354	# define EV_USE_4HEAP EV_FEATURE_DATA	380	# define EV_USE_4HEAP EV_FEATURE_DATA
355	#endif	381	#endif
356		382
357	#ifndef EV_HEAP_CACHE_AT	383	#ifndef EV_HEAP_CACHE_AT
358	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA	384	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA
		385	#endif
		386
		387	#ifdef __ANDROID__
		388	/* supposedly, android doesn't typedef fd_mask */
		389	# undef EV_USE_SELECT
		390	# define EV_USE_SELECT 0
		391	/* supposedly, we need to include syscall.h, not sys/syscall.h, so just disable */
		392	# undef EV_USE_CLOCK_SYSCALL
		393	# define EV_USE_CLOCK_SYSCALL 0
		394	#endif
		395
		396	/* aix's poll.h seems to cause lots of trouble */
		397	#ifdef _AIX
		398	/* AIX has a completely broken poll.h header */
		399	# undef EV_USE_POLL
		400	# define EV_USE_POLL 0
359	#endif	401	#endif
360		402
361	/* on linux, we can use a (slow) syscall to avoid a dependency on pthread, */	403	/* on linux, we can use a (slow) syscall to avoid a dependency on pthread, */
362	/* which makes programs even slower. might work on other unices, too. */	404	/* which makes programs even slower. might work on other unices, too. */
363	#if EV_USE_CLOCK_SYSCALL	405	#if EV_USE_CLOCK_SYSCALL
…		…
372	# endif	414	# endif
373	#endif	415	#endif
374		416
375	/* this block fixes any misconfiguration where we know we run into trouble otherwise */	417	/* this block fixes any misconfiguration where we know we run into trouble otherwise */
376		418
377	#ifdef _AIX
378	/* AIX has a completely broken poll.h header */
379	# undef EV_USE_POLL
380	# define EV_USE_POLL 0
381	#endif
382
383	#ifndef CLOCK_MONOTONIC	419	#ifndef CLOCK_MONOTONIC
384	# undef EV_USE_MONOTONIC	420	# undef EV_USE_MONOTONIC
385	# define EV_USE_MONOTONIC 0	421	# define EV_USE_MONOTONIC 0
386	#endif	422	#endif
387		423
…		…
397		433
398	#if !EV_USE_NANOSLEEP	434	#if !EV_USE_NANOSLEEP
399	/* hp-ux has it in sys/time.h, which we unconditionally include above */	435	/* hp-ux has it in sys/time.h, which we unconditionally include above */
400	# if !defined _WIN32 && !defined __hpux	436	# if !defined _WIN32 && !defined __hpux
401	# include <sys/select.h>	437	# include <sys/select.h>
		438	# endif
		439	#endif
		440
		441	#if EV_USE_LINUXAIO
		442	# include <sys/syscall.h>
		443	# if !SYS_io_getevents || !EV_USE_EPOLL /* ev_linxaio uses ev_poll.c:ev_epoll_create */
		444	# undef EV_USE_LINUXAIO
		445	# define EV_USE_LINUXAIO 0
402	# endif	446	# endif
403	#endif	447	#endif
404		448
405	#if EV_USE_INOTIFY	449	#if EV_USE_INOTIFY
406	# include <sys/statfs.h>	450	# include <sys/statfs.h>
…		…
408	/* some very old inotify.h headers don't have IN_DONT_FOLLOW */	452	/* some very old inotify.h headers don't have IN_DONT_FOLLOW */
409	# ifndef IN_DONT_FOLLOW	453	# ifndef IN_DONT_FOLLOW
410	# undef EV_USE_INOTIFY	454	# undef EV_USE_INOTIFY
411	# define EV_USE_INOTIFY 0	455	# define EV_USE_INOTIFY 0
412	# endif	456	# endif
413	#endif
414
415	#if EV_SELECT_IS_WINSOCKET
416	# include <winsock.h>
417	#endif	457	#endif
418		458
419	#if EV_USE_EVENTFD	459	#if EV_USE_EVENTFD
420	/* our minimum requirement is glibc 2.7 which has the stub, but not the header */	460	/* our minimum requirement is glibc 2.7 which has the stub, but not the header */
421	# include <stdint.h>	461	# include <stdint.h>
…		…
478	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */	518	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */
479	/* ECB.H BEGIN */	519	/* ECB.H BEGIN */
480	/*	520	/*
481	* libecb - http://software.schmorp.de/pkg/libecb	521	* libecb - http://software.schmorp.de/pkg/libecb
482	*	522	*
483	* Copyright (©) 2009-2012 Marc Alexander Lehmann <libecb@schmorp.de>	523	* Copyright (©) 2009-2015 Marc Alexander Lehmann <libecb@schmorp.de>
484	* Copyright (©) 2011 Emanuele Giaquinta	524	* Copyright (©) 2011 Emanuele Giaquinta
485	* All rights reserved.	525	* All rights reserved.
486	*	526	*
487	* Redistribution and use in source and binary forms, with or without modifica-	527	* Redistribution and use in source and binary forms, with or without modifica-
488	* tion, are permitted provided that the following conditions are met:	528	* tion, are permitted provided that the following conditions are met:
…		…
502	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;	542	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;
503	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,	543	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,
504	* WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING NEGLIGENCE OR OTH-	544	* WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING NEGLIGENCE OR OTH-
505	* ERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED	545	* ERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED
506	* OF THE POSSIBILITY OF SUCH DAMAGE.	546	* OF THE POSSIBILITY OF SUCH DAMAGE.
		547	*
		548	* Alternatively, the contents of this file may be used under the terms of
		549	* the GNU General Public License ("GPL") version 2 or any later version,
		550	* in which case the provisions of the GPL are applicable instead of
		551	* the above. If you wish to allow the use of your version of this file
		552	* only under the terms of the GPL and not to allow others to use your
		553	* version of this file under the BSD license, indicate your decision
		554	* by deleting the provisions above and replace them with the notice
		555	* and other provisions required by the GPL. If you do not delete the
		556	* provisions above, a recipient may use your version of this file under
		557	* either the BSD or the GPL.
507	*/	558	*/
508		559
509	#ifndef ECB_H	560	#ifndef ECB_H
510	#define ECB_H	561	#define ECB_H
		562
		563	/* 16 bits major, 16 bits minor */
		564	#define ECB_VERSION 0x00010006
511		565
512	#ifdef _WIN32	566	#ifdef _WIN32
513	typedef signed char int8_t;	567	typedef signed char int8_t;
514	typedef unsigned char uint8_t;	568	typedef unsigned char uint8_t;
515	typedef signed short int16_t;	569	typedef signed short int16_t;
…		…
521	typedef unsigned long long uint64_t;	575	typedef unsigned long long uint64_t;
522	#else /* _MSC_VER || __BORLANDC__ */	576	#else /* _MSC_VER || __BORLANDC__ */
523	typedef signed __int64 int64_t;	577	typedef signed __int64 int64_t;
524	typedef unsigned __int64 uint64_t;	578	typedef unsigned __int64 uint64_t;
525	#endif	579	#endif
		580	#ifdef _WIN64
		581	#define ECB_PTRSIZE 8
		582	typedef uint64_t uintptr_t;
		583	typedef int64_t intptr_t;
		584	#else
		585	#define ECB_PTRSIZE 4
		586	typedef uint32_t uintptr_t;
		587	typedef int32_t intptr_t;
		588	#endif
526	#else	589	#else
527	#include <inttypes.h>	590	#include <inttypes.h>
		591	#if (defined INTPTR_MAX ? INTPTR_MAX : ULONG_MAX) > 0xffffffffU
		592	#define ECB_PTRSIZE 8
		593	#else
		594	#define ECB_PTRSIZE 4
		595	#endif
		596	#endif
		597
		598	#define ECB_GCC_AMD64 (__amd64 || __amd64__ || __x86_64 || __x86_64__)
		599	#define ECB_MSVC_AMD64 (_M_AMD64 || _M_X64)
		600
		601	/* work around x32 idiocy by defining proper macros */
		602	#if ECB_GCC_AMD64 || ECB_MSVC_AMD64
		603	#if _ILP32
		604	#define ECB_AMD64_X32 1
		605	#else
		606	#define ECB_AMD64 1
		607	#endif
528	#endif	608	#endif
529		609
530	/* many compilers define _GNUC_ to some versions but then only implement	610	/* many compilers define _GNUC_ to some versions but then only implement
531	* what their idiot authors think are the "more important" extensions,	611	* what their idiot authors think are the "more important" extensions,
532	* causing enormous grief in return for some better fake benchmark numbers.	612	* causing enormous grief in return for some better fake benchmark numbers.
533	* or so.	613	* or so.
534	* we try to detect these and simply assume they are not gcc - if they have	614	* we try to detect these and simply assume they are not gcc - if they have
535	* an issue with that they should have done it right in the first place.	615	* an issue with that they should have done it right in the first place.
536	*/	616	*/
537	#ifndef ECB_GCC_VERSION
538	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__	617	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__
539	#define ECB_GCC_VERSION(major,minor) 0	618	#define ECB_GCC_VERSION(major,minor) 0
540	#else	619	#else
541	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))	620	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))
542	#endif	621	#endif
		622
		623	#define ECB_CLANG_VERSION(major,minor) (__clang_major__ > (major) || (__clang_major__ == (major) && __clang_minor__ >= (minor)))
		624
		625	#if __clang__ && defined __has_builtin
		626	#define ECB_CLANG_BUILTIN(x) __has_builtin (x)
		627	#else
		628	#define ECB_CLANG_BUILTIN(x) 0
		629	#endif
		630
		631	#if __clang__ && defined __has_extension
		632	#define ECB_CLANG_EXTENSION(x) __has_extension (x)
		633	#else
		634	#define ECB_CLANG_EXTENSION(x) 0
		635	#endif
		636
		637	#define ECB_CPP (__cplusplus+0)
		638	#define ECB_CPP11 (__cplusplus >= 201103L)
		639	#define ECB_CPP14 (__cplusplus >= 201402L)
		640	#define ECB_CPP17 (__cplusplus >= 201703L)
		641
		642	#if ECB_CPP
		643	#define ECB_C 0
		644	#define ECB_STDC_VERSION 0
		645	#else
		646	#define ECB_C 1
		647	#define ECB_STDC_VERSION __STDC_VERSION__
		648	#endif
		649
		650	#define ECB_C99 (ECB_STDC_VERSION >= 199901L)
		651	#define ECB_C11 (ECB_STDC_VERSION >= 201112L)
		652	#define ECB_C17 (ECB_STDC_VERSION >= 201710L)
		653
		654	#if ECB_CPP
		655	#define ECB_EXTERN_C extern "C"
		656	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {
		657	#define ECB_EXTERN_C_END }
		658	#else
		659	#define ECB_EXTERN_C extern
		660	#define ECB_EXTERN_C_BEG
		661	#define ECB_EXTERN_C_END
543	#endif	662	#endif
544		663
545	/*****************************************************************************/	664	/*****************************************************************************/
546		665
547	/* ECB_NO_THREADS - ecb is not used by multiple threads, ever */	666	/* ECB_NO_THREADS - ecb is not used by multiple threads, ever */
548	/* ECB_NO_SMP - ecb might be used in multiple threads, but only on a single cpu */	667	/* ECB_NO_SMP - ecb might be used in multiple threads, but only on a single cpu */
549		668
550	#if ECB_NO_THREADS	669	#if ECB_NO_THREADS
551	# define ECB_NO_SMP 1	670	#define ECB_NO_SMP 1
552	#endif	671	#endif
553		672
554	#if ECB_NO_THREADS || ECB_NO_SMP	673	#if ECB_NO_SMP
555	#define ECB_MEMORY_FENCE do { } while (0)	674	#define ECB_MEMORY_FENCE do { } while (0)
		675	#endif
		676
		677	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/compiler_ref/compiler_builtins.html */
		678	#if __xlC__ && ECB_CPP
		679	#include <builtins.h>
		680	#endif
		681
		682	#if 1400 <= _MSC_VER
		683	#include <intrin.h> /* fence functions _ReadBarrier, also bit search functions _BitScanReverse */
556	#endif	684	#endif
557		685
558	#ifndef ECB_MEMORY_FENCE	686	#ifndef ECB_MEMORY_FENCE
559	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	687	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
		688	#define ECB_MEMORY_FENCE_RELAXED __asm__ __volatile__ ("" : : : "memory")
560	#if __i386 || __i386__	689	#if __i386 || __i386__
561	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")	690	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")
562	#define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE /* non-lock xchg might be enough */	691	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
563	#define ECB_MEMORY_FENCE_RELEASE do { } while (0) /* unlikely to change in future cpus */	692	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
564	#elif __amd64 || __amd64__ || __x86_64 || __x86_64__	693	#elif ECB_GCC_AMD64
565	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")	694	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")
566	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("lfence" : : : "memory")	695	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
567	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("sfence") /* play safe - not needed in any current cpu */	696	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
568	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__	697	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__
569	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")	698	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")
		699	#elif defined __ARM_ARCH_2__ \
		700	|| defined __ARM_ARCH_3__ || defined __ARM_ARCH_3M__ \
		701	|| defined __ARM_ARCH_4__ || defined __ARM_ARCH_4T__ \
		702	|| defined __ARM_ARCH_5__ || defined __ARM_ARCH_5E__ \
		703	|| defined __ARM_ARCH_5T__ || defined __ARM_ARCH_5TE__ \
		704	|| defined __ARM_ARCH_5TEJ__
		705	/* should not need any, unless running old code on newer cpu - arm doesn't support that */
570	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \	706	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \
571	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__	707	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__ \
		708	|| defined __ARM_ARCH_6T2__
572	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")	709	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")
573	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \	710	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \
574	|| defined __ARM_ARCH_7M__ || defined __ARM_ARCH_7R__	711	|| defined __ARM_ARCH_7R__ || defined __ARM_ARCH_7M__
575	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")	712	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")
576	#elif __sparc || __sparc__	713	#elif __aarch64__
		714	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb ish" : : : "memory")
		715	#elif (__sparc || __sparc__) && !(__sparc_v8__ || defined __sparcv8)
577	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad | " : : : "memory")	716	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")
578	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")	717	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")
579	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")	718	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")
580	#elif defined __s390__ || defined __s390x__	719	#elif defined __s390__ || defined __s390x__
581	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")	720	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")
582	#elif defined __mips__	721	#elif defined __mips__
		722	/* GNU/Linux emulates sync on mips1 architectures, so we force its use */
		723	/* anybody else who still uses mips1 is supposed to send in their version, with detection code. */
583	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")	724	#define ECB_MEMORY_FENCE __asm__ __volatile__ (".set mips2; sync; .set mips0" : : : "memory")
584	#elif defined __alpha__	725	#elif defined __alpha__
585	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mb" : : : "memory")	726	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mb" : : : "memory")
		727	#elif defined __hppa__
		728	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("" : : : "memory")
		729	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")
		730	#elif defined __ia64__
		731	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mf" : : : "memory")
		732	#elif defined __m68k__
		733	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("" : : : "memory")
		734	#elif defined __m88k__
		735	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("tb1 0,%%r0,128" : : : "memory")
		736	#elif defined __sh__
		737	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("" : : : "memory")
586	#endif	738	#endif
587	#endif	739	#endif
588	#endif	740	#endif
589		741
590	#ifndef ECB_MEMORY_FENCE	742	#ifndef ECB_MEMORY_FENCE
		743	#if ECB_GCC_VERSION(4,7)
		744	/* see comment below (stdatomic.h) about the C11 memory model. */
		745	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)
		746	#define ECB_MEMORY_FENCE_ACQUIRE __atomic_thread_fence (__ATOMIC_ACQUIRE)
		747	#define ECB_MEMORY_FENCE_RELEASE __atomic_thread_fence (__ATOMIC_RELEASE)
		748	#define ECB_MEMORY_FENCE_RELAXED __atomic_thread_fence (__ATOMIC_RELAXED)
		749
		750	#elif ECB_CLANG_EXTENSION(c_atomic)
		751	/* see comment below (stdatomic.h) about the C11 memory model. */
		752	#define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)
		753	#define ECB_MEMORY_FENCE_ACQUIRE __c11_atomic_thread_fence (__ATOMIC_ACQUIRE)
		754	#define ECB_MEMORY_FENCE_RELEASE __c11_atomic_thread_fence (__ATOMIC_RELEASE)
		755	#define ECB_MEMORY_FENCE_RELAXED __c11_atomic_thread_fence (__ATOMIC_RELAXED)
		756
591	#if ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__	757	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__
592	#define ECB_MEMORY_FENCE __sync_synchronize ()	758	#define ECB_MEMORY_FENCE __sync_synchronize ()
593	/*#define ECB_MEMORY_FENCE_ACQUIRE ({ char dummy = 0; __sync_lock_test_and_set (&dummy, 1); }) */	759	#elif _MSC_VER >= 1500 /* VC++ 2008 */
594	/*#define ECB_MEMORY_FENCE_RELEASE ({ char dummy = 1; __sync_lock_release (&dummy ); }) */	760	/* apparently, microsoft broke all the memory barrier stuff in Visual Studio 2008... */
		761	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)
		762	#define ECB_MEMORY_FENCE _ReadWriteBarrier (); MemoryBarrier()
		763	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier (); MemoryBarrier() /* according to msdn, _ReadBarrier is not a load fence */
		764	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier (); MemoryBarrier()
595	#elif _MSC_VER >= 1400 /* VC++ 2005 */	765	#elif _MSC_VER >= 1400 /* VC++ 2005 */
596	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)	766	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)
597	#define ECB_MEMORY_FENCE _ReadWriteBarrier ()	767	#define ECB_MEMORY_FENCE _ReadWriteBarrier ()
598	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier () /* according to msdn, _ReadBarrier is not a load fence */	768	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier () /* according to msdn, _ReadBarrier is not a load fence */
599	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier ()	769	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier ()
600	#elif defined _WIN32	770	#elif defined _WIN32
601	#include <WinNT.h>	771	#include <WinNT.h>
602	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */	772	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */
603	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	773	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
604	#include <mbarrier.h>	774	#include <mbarrier.h>
605	#define ECB_MEMORY_FENCE __machine_rw_barrier ()	775	#define ECB_MEMORY_FENCE __machine_rw_barrier ()
606	#define ECB_MEMORY_FENCE_ACQUIRE __machine_r_barrier ()	776	#define ECB_MEMORY_FENCE_ACQUIRE __machine_acq_barrier ()
607	#define ECB_MEMORY_FENCE_RELEASE __machine_w_barrier ()	777	#define ECB_MEMORY_FENCE_RELEASE __machine_rel_barrier ()
		778	#define ECB_MEMORY_FENCE_RELAXED __compiler_barrier ()
608	#elif __xlC__	779	#elif __xlC__
609	#define ECB_MEMORY_FENCE __sync ()	780	#define ECB_MEMORY_FENCE __sync ()
		781	#endif
		782	#endif
		783
		784	#ifndef ECB_MEMORY_FENCE
		785	#if ECB_C11 && !defined __STDC_NO_ATOMICS__
		786	/* we assume that these memory fences work on all variables/all memory accesses, */
		787	/* not just C11 atomics and atomic accesses */
		788	#include <stdatomic.h>
		789	#define ECB_MEMORY_FENCE atomic_thread_fence (memory_order_seq_cst)
		790	#define ECB_MEMORY_FENCE_ACQUIRE atomic_thread_fence (memory_order_acquire)
		791	#define ECB_MEMORY_FENCE_RELEASE atomic_thread_fence (memory_order_release)
610	#endif	792	#endif
611	#endif	793	#endif
612		794
613	#ifndef ECB_MEMORY_FENCE	795	#ifndef ECB_MEMORY_FENCE
614	#if !ECB_AVOID_PTHREADS	796	#if !ECB_AVOID_PTHREADS
…		…
634		816
635	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE	817	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE
636	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	818	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
637	#endif	819	#endif
638		820
		821	#if !defined ECB_MEMORY_FENCE_RELAXED && defined ECB_MEMORY_FENCE
		822	#define ECB_MEMORY_FENCE_RELAXED ECB_MEMORY_FENCE /* very heavy-handed */
		823	#endif
		824
639	/*****************************************************************************/	825	/*****************************************************************************/
640		826
641	#define ECB_C99 (__STDC_VERSION__ >= 199901L)	827	#if ECB_CPP
642
643	#if __cplusplus
644	#define ecb_inline static inline	828	#define ecb_inline static inline
645	#elif ECB_GCC_VERSION(2,5)	829	#elif ECB_GCC_VERSION(2,5)
646	#define ecb_inline static __inline__	830	#define ecb_inline static __inline__
647	#elif ECB_C99	831	#elif ECB_C99
648	#define ecb_inline static inline	832	#define ecb_inline static inline
…		…
662		846
663	#define ECB_CONCAT_(a, b) a ## b	847	#define ECB_CONCAT_(a, b) a ## b
664	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)	848	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)
665	#define ECB_STRINGIFY_(a) # a	849	#define ECB_STRINGIFY_(a) # a
666	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)	850	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)
		851	#define ECB_STRINGIFY_EXPR(expr) ((expr), ECB_STRINGIFY_ (expr))
667		852
668	#define ecb_function_ ecb_inline	853	#define ecb_function_ ecb_inline
669		854
670	#if ECB_GCC_VERSION(3,1)	855	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_VERSION(2,8)
671	#define ecb_attribute(attrlist) __attribute__(attrlist)	856	#define ecb_attribute(attrlist) __attribute__ (attrlist)
		857	#else
		858	#define ecb_attribute(attrlist)
		859	#endif
		860
		861	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_constant_p)
672	#define ecb_is_constant(expr) __builtin_constant_p (expr)	862	#define ecb_is_constant(expr) __builtin_constant_p (expr)
		863	#else
		864	/* possible C11 impl for integral types
		865	typedef struct ecb_is_constant_struct ecb_is_constant_struct;
		866	#define ecb_is_constant(expr) _Generic ((1 ? (struct ecb_is_constant_struct *)0 : (void *)((expr) - (expr)), ecb_is_constant_struct *: 0, default: 1)) */
		867
		868	#define ecb_is_constant(expr) 0
		869	#endif
		870
		871	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_expect)
673	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))	872	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))
		873	#else
		874	#define ecb_expect(expr,value) (expr)
		875	#endif
		876
		877	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_prefetch)
674	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)	878	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)
675	#else	879	#else
676	#define ecb_attribute(attrlist)
677	#define ecb_is_constant(expr) 0
678	#define ecb_expect(expr,value) (expr)
679	#define ecb_prefetch(addr,rw,locality)	880	#define ecb_prefetch(addr,rw,locality)
680	#endif	881	#endif
681		882
682	/* no emulation for ecb_decltype */	883	/* no emulation for ecb_decltype */
683	#if ECB_GCC_VERSION(4,5)	884	#if ECB_CPP11
		885	// older implementations might have problems with decltype(x)::type, work around it
		886	template<class T> struct ecb_decltype_t { typedef T type; };
684	#define ecb_decltype(x) __decltype(x)	887	#define ecb_decltype(x) ecb_decltype_t<decltype (x)>::type
685	#elif ECB_GCC_VERSION(3,0)	888	#elif ECB_GCC_VERSION(3,0) || ECB_CLANG_VERSION(2,8)
686	#define ecb_decltype(x) __typeof(x)	889	#define ecb_decltype(x) __typeof__ (x)
687	#endif	890	#endif
688		891
		892	#if _MSC_VER >= 1300
		893	#define ecb_deprecated __declspec (deprecated)
		894	#else
		895	#define ecb_deprecated ecb_attribute ((__deprecated__))
		896	#endif
		897
		898	#if _MSC_VER >= 1500
		899	#define ecb_deprecated_message(msg) __declspec (deprecated (msg))
		900	#elif ECB_GCC_VERSION(4,5)
		901	#define ecb_deprecated_message(msg) ecb_attribute ((__deprecated__ (msg))
		902	#else
		903	#define ecb_deprecated_message(msg) ecb_deprecated
		904	#endif
		905
		906	#if _MSC_VER >= 1400
		907	#define ecb_noinline __declspec (noinline)
		908	#else
689	#define ecb_noinline ecb_attribute ((__noinline__))	909	#define ecb_noinline ecb_attribute ((__noinline__))
690	#define ecb_noreturn ecb_attribute ((__noreturn__))	910	#endif
		911
691	#define ecb_unused ecb_attribute ((__unused__))	912	#define ecb_unused ecb_attribute ((__unused__))
692	#define ecb_const ecb_attribute ((__const__))	913	#define ecb_const ecb_attribute ((__const__))
693	#define ecb_pure ecb_attribute ((__pure__))	914	#define ecb_pure ecb_attribute ((__pure__))
		915
		916	#if ECB_C11 || __IBMC_NORETURN
		917	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/language_ref/noreturn.html */
		918	#define ecb_noreturn _Noreturn
		919	#elif ECB_CPP11
		920	#define ecb_noreturn [[noreturn]]
		921	#elif _MSC_VER >= 1200
		922	/* http://msdn.microsoft.com/en-us/library/k6ktzx3s.aspx */
		923	#define ecb_noreturn __declspec (noreturn)
		924	#else
		925	#define ecb_noreturn ecb_attribute ((__noreturn__))
		926	#endif
694		927
695	#if ECB_GCC_VERSION(4,3)	928	#if ECB_GCC_VERSION(4,3)
696	#define ecb_artificial ecb_attribute ((__artificial__))	929	#define ecb_artificial ecb_attribute ((__artificial__))
697	#define ecb_hot ecb_attribute ((__hot__))	930	#define ecb_hot ecb_attribute ((__hot__))
698	#define ecb_cold ecb_attribute ((__cold__))	931	#define ecb_cold ecb_attribute ((__cold__))
…		…
710	/* for compatibility to the rest of the world */	943	/* for compatibility to the rest of the world */
711	#define ecb_likely(expr) ecb_expect_true (expr)	944	#define ecb_likely(expr) ecb_expect_true (expr)
712	#define ecb_unlikely(expr) ecb_expect_false (expr)	945	#define ecb_unlikely(expr) ecb_expect_false (expr)
713		946
714	/* count trailing zero bits and count # of one bits */	947	/* count trailing zero bits and count # of one bits */
715	#if ECB_GCC_VERSION(3,4)	948	#if ECB_GCC_VERSION(3,4) \
		949	|| (ECB_CLANG_BUILTIN(__builtin_clz) && ECB_CLANG_BUILTIN(__builtin_clzll) \
		950	&& ECB_CLANG_BUILTIN(__builtin_ctz) && ECB_CLANG_BUILTIN(__builtin_ctzll) \
		951	&& ECB_CLANG_BUILTIN(__builtin_popcount))
716	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */	952	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */
717	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)	953	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)
718	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)	954	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)
719	#define ecb_ctz32(x) __builtin_ctz (x)	955	#define ecb_ctz32(x) __builtin_ctz (x)
720	#define ecb_ctz64(x) __builtin_ctzll (x)	956	#define ecb_ctz64(x) __builtin_ctzll (x)
721	#define ecb_popcount32(x) __builtin_popcount (x)	957	#define ecb_popcount32(x) __builtin_popcount (x)
722	/* no popcountll */	958	/* no popcountll */
723	#else	959	#else
724	ecb_function_ int ecb_ctz32 (uint32_t x) ecb_const;	960	ecb_function_ ecb_const int ecb_ctz32 (uint32_t x);
725	ecb_function_ int	961	ecb_function_ ecb_const int
726	ecb_ctz32 (uint32_t x)	962	ecb_ctz32 (uint32_t x)
727	{	963	{
		964	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		965	unsigned long r;
		966	_BitScanForward (&r, x);
		967	return (int)r;
		968	#else
728	int r = 0;	969	int r = 0;
729		970
730	x &= ~x + 1; /* this isolates the lowest bit */	971	x &= ~x + 1; /* this isolates the lowest bit */
731		972
732	#if ECB_branchless_on_i386	973	#if ECB_branchless_on_i386
…		…
742	if (x & 0xff00ff00) r += 8;	983	if (x & 0xff00ff00) r += 8;
743	if (x & 0xffff0000) r += 16;	984	if (x & 0xffff0000) r += 16;
744	#endif	985	#endif
745		986
746	return r;	987	return r;
		988	#endif
747	}	989	}
748		990
749	ecb_function_ int ecb_ctz64 (uint64_t x) ecb_const;	991	ecb_function_ ecb_const int ecb_ctz64 (uint64_t x);
750	ecb_function_ int	992	ecb_function_ ecb_const int
751	ecb_ctz64 (uint64_t x)	993	ecb_ctz64 (uint64_t x)
752	{	994	{
		995	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		996	unsigned long r;
		997	_BitScanForward64 (&r, x);
		998	return (int)r;
		999	#else
753	int shift = x & 0xffffffffU ? 0 : 32;	1000	int shift = x & 0xffffffff ? 0 : 32;
754	return ecb_ctz32 (x >> shift) + shift;	1001	return ecb_ctz32 (x >> shift) + shift;
		1002	#endif
755	}	1003	}
756		1004
757	ecb_function_ int ecb_popcount32 (uint32_t x) ecb_const;	1005	ecb_function_ ecb_const int ecb_popcount32 (uint32_t x);
758	ecb_function_ int	1006	ecb_function_ ecb_const int
759	ecb_popcount32 (uint32_t x)	1007	ecb_popcount32 (uint32_t x)
760	{	1008	{
761	x -= (x >> 1) & 0x55555555;	1009	x -= (x >> 1) & 0x55555555;
762	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);	1010	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);
763	x = ((x >> 4) + x) & 0x0f0f0f0f;	1011	x = ((x >> 4) + x) & 0x0f0f0f0f;
764	x *= 0x01010101;	1012	x *= 0x01010101;
765		1013
766	return x >> 24;	1014	return x >> 24;
767	}	1015	}
768		1016
769	ecb_function_ int ecb_ld32 (uint32_t x) ecb_const;	1017	ecb_function_ ecb_const int ecb_ld32 (uint32_t x);
770	ecb_function_ int ecb_ld32 (uint32_t x)	1018	ecb_function_ ecb_const int ecb_ld32 (uint32_t x)
771	{	1019	{
		1020	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		1021	unsigned long r;
		1022	_BitScanReverse (&r, x);
		1023	return (int)r;
		1024	#else
772	int r = 0;	1025	int r = 0;
773		1026
774	if (x >> 16) { x >>= 16; r += 16; }	1027	if (x >> 16) { x >>= 16; r += 16; }
775	if (x >> 8) { x >>= 8; r += 8; }	1028	if (x >> 8) { x >>= 8; r += 8; }
776	if (x >> 4) { x >>= 4; r += 4; }	1029	if (x >> 4) { x >>= 4; r += 4; }
777	if (x >> 2) { x >>= 2; r += 2; }	1030	if (x >> 2) { x >>= 2; r += 2; }
778	if (x >> 1) { r += 1; }	1031	if (x >> 1) { r += 1; }
779		1032
780	return r;	1033	return r;
		1034	#endif
781	}	1035	}
782		1036
783	ecb_function_ int ecb_ld64 (uint64_t x) ecb_const;	1037	ecb_function_ ecb_const int ecb_ld64 (uint64_t x);
784	ecb_function_ int ecb_ld64 (uint64_t x)	1038	ecb_function_ ecb_const int ecb_ld64 (uint64_t x)
785	{	1039	{
		1040	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1041	unsigned long r;
		1042	_BitScanReverse64 (&r, x);
		1043	return (int)r;
		1044	#else
786	int r = 0;	1045	int r = 0;
787		1046
788	if (x >> 32) { x >>= 32; r += 32; }	1047	if (x >> 32) { x >>= 32; r += 32; }
789		1048
790	return r + ecb_ld32 (x);	1049	return r + ecb_ld32 (x);
		1050	#endif
791	}	1051	}
792	#endif	1052	#endif
793		1053
		1054	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x);
		1055	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x) { return !(x & (x - 1)); }
		1056	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x);
		1057	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x) { return !(x & (x - 1)); }
		1058
794	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x) ecb_const;	1059	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x);
795	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x)	1060	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x)
796	{	1061	{
797	return ( (x * 0x0802U & 0x22110U)	1062	return ( (x * 0x0802U & 0x22110U)
798	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;	1063	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;
799	}	1064	}
800		1065
801	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x) ecb_const;	1066	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x);
802	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x)	1067	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x)
803	{	1068	{
804	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);	1069	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);
805	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);	1070	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);
806	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);	1071	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);
807	x = ( x >> 8 ) | ( x << 8);	1072	x = ( x >> 8 ) | ( x << 8);
808		1073
809	return x;	1074	return x;
810	}	1075	}
811		1076
812	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x) ecb_const;	1077	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x);
813	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x)	1078	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x)
814	{	1079	{
815	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);	1080	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);
816	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);	1081	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);
817	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);	1082	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);
818	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);	1083	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);
…		…
821	return x;	1086	return x;
822	}	1087	}
823		1088
824	/* popcount64 is only available on 64 bit cpus as gcc builtin */	1089	/* popcount64 is only available on 64 bit cpus as gcc builtin */
825	/* so for this version we are lazy */	1090	/* so for this version we are lazy */
826	ecb_function_ int ecb_popcount64 (uint64_t x) ecb_const;	1091	ecb_function_ ecb_const int ecb_popcount64 (uint64_t x);
827	ecb_function_ int	1092	ecb_function_ ecb_const int
828	ecb_popcount64 (uint64_t x)	1093	ecb_popcount64 (uint64_t x)
829	{	1094	{
830	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);	1095	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);
831	}	1096	}
832		1097
833	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) ecb_const;	1098	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count);
834	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) ecb_const;	1099	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count);
835	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) ecb_const;	1100	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count);
836	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) ecb_const;	1101	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count);
837	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) ecb_const;	1102	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count);
838	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) ecb_const;	1103	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count);
839	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) ecb_const;	1104	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count);
840	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) ecb_const;	1105	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count);
841		1106
842	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }	1107	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }
843	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }	1108	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }
844	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }	1109	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }
845	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }	1110	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }
846	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }	1111	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }
847	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }	1112	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }
848	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }	1113	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }
849	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }	1114	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }
850		1115
851	#if ECB_GCC_VERSION(4,3)	1116	#if ECB_GCC_VERSION(4,3) || (ECB_CLANG_BUILTIN(__builtin_bswap32) && ECB_CLANG_BUILTIN(__builtin_bswap64))
		1117	#if ECB_GCC_VERSION(4,8) || ECB_CLANG_BUILTIN(__builtin_bswap16)
		1118	#define ecb_bswap16(x) __builtin_bswap16 (x)
		1119	#else
852	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)	1120	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)
		1121	#endif
853	#define ecb_bswap32(x) __builtin_bswap32 (x)	1122	#define ecb_bswap32(x) __builtin_bswap32 (x)
854	#define ecb_bswap64(x) __builtin_bswap64 (x)	1123	#define ecb_bswap64(x) __builtin_bswap64 (x)
		1124	#elif _MSC_VER
		1125	#include <stdlib.h>
		1126	#define ecb_bswap16(x) ((uint16_t)_byteswap_ushort ((uint16_t)(x)))
		1127	#define ecb_bswap32(x) ((uint32_t)_byteswap_ulong ((uint32_t)(x)))
		1128	#define ecb_bswap64(x) ((uint64_t)_byteswap_uint64 ((uint64_t)(x)))
855	#else	1129	#else
856	ecb_function_ uint16_t ecb_bswap16 (uint16_t x) ecb_const;	1130	ecb_function_ ecb_const uint16_t ecb_bswap16 (uint16_t x);
857	ecb_function_ uint16_t	1131	ecb_function_ ecb_const uint16_t
858	ecb_bswap16 (uint16_t x)	1132	ecb_bswap16 (uint16_t x)
859	{	1133	{
860	return ecb_rotl16 (x, 8);	1134	return ecb_rotl16 (x, 8);
861	}	1135	}
862		1136
863	ecb_function_ uint32_t ecb_bswap32 (uint32_t x) ecb_const;	1137	ecb_function_ ecb_const uint32_t ecb_bswap32 (uint32_t x);
864	ecb_function_ uint32_t	1138	ecb_function_ ecb_const uint32_t
865	ecb_bswap32 (uint32_t x)	1139	ecb_bswap32 (uint32_t x)
866	{	1140	{
867	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);	1141	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);
868	}	1142	}
869		1143
870	ecb_function_ uint64_t ecb_bswap64 (uint64_t x) ecb_const;	1144	ecb_function_ ecb_const uint64_t ecb_bswap64 (uint64_t x);
871	ecb_function_ uint64_t	1145	ecb_function_ ecb_const uint64_t
872	ecb_bswap64 (uint64_t x)	1146	ecb_bswap64 (uint64_t x)
873	{	1147	{
874	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);	1148	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);
875	}	1149	}
876	#endif	1150	#endif
877		1151
878	#if ECB_GCC_VERSION(4,5)	1152	#if ECB_GCC_VERSION(4,5) || ECB_CLANG_BUILTIN(__builtin_unreachable)
879	#define ecb_unreachable() __builtin_unreachable ()	1153	#define ecb_unreachable() __builtin_unreachable ()
880	#else	1154	#else
881	/* this seems to work fine, but gcc always emits a warning for it :/ */	1155	/* this seems to work fine, but gcc always emits a warning for it :/ */
882	ecb_inline void ecb_unreachable (void) ecb_noreturn;	1156	ecb_inline ecb_noreturn void ecb_unreachable (void);
883	ecb_inline void ecb_unreachable (void) { }	1157	ecb_inline ecb_noreturn void ecb_unreachable (void) { }
884	#endif	1158	#endif
885		1159
886	/* try to tell the compiler that some condition is definitely true */	1160	/* try to tell the compiler that some condition is definitely true */
887	#define ecb_assume(cond) do { if (!(cond)) ecb_unreachable (); } while (0)	1161	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0
888		1162
889	ecb_inline unsigned char ecb_byteorder_helper (void) ecb_const;	1163	ecb_inline ecb_const uint32_t ecb_byteorder_helper (void);
890	ecb_inline unsigned char	1164	ecb_inline ecb_const uint32_t
891	ecb_byteorder_helper (void)	1165	ecb_byteorder_helper (void)
892	{	1166	{
893	const uint32_t u = 0x11223344;	1167	/* the union code still generates code under pressure in gcc, */
894	return *(unsigned char *)&u;	1168	/* but less than using pointers, and always seems to */
		1169	/* successfully return a constant. */
		1170	/* the reason why we have this horrible preprocessor mess */
		1171	/* is to avoid it in all cases, at least on common architectures */
		1172	/* or when using a recent enough gcc version (>= 4.6) */
		1173	#if (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_LITTLE_ENDIAN__) \
		1174	|| ((__i386 || __i386__ || _M_IX86 || ECB_GCC_AMD64 || ECB_MSVC_AMD64) && !__VOS__)
		1175	#define ECB_LITTLE_ENDIAN 1
		1176	return 0x44332211;
		1177	#elif (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__) \
		1178	|| ((__AARCH64EB__ || __MIPSEB__ || __ARMEB__) && !__VOS__)
		1179	#define ECB_BIG_ENDIAN 1
		1180	return 0x11223344;
		1181	#else
		1182	union
		1183	{
		1184	uint8_t c[4];
		1185	uint32_t u;
		1186	} u = { 0x11, 0x22, 0x33, 0x44 };
		1187	return u.u;
		1188	#endif
895	}	1189	}
896		1190
897	ecb_inline ecb_bool ecb_big_endian (void) ecb_const;	1191	ecb_inline ecb_const ecb_bool ecb_big_endian (void);
898	ecb_inline ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11; }	1192	ecb_inline ecb_const ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11223344; }
899	ecb_inline ecb_bool ecb_little_endian (void) ecb_const;	1193	ecb_inline ecb_const ecb_bool ecb_little_endian (void);
900	ecb_inline ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44; }	1194	ecb_inline ecb_const ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44332211; }
901		1195
902	#if ECB_GCC_VERSION(3,0) || ECB_C99	1196	#if ECB_GCC_VERSION(3,0) || ECB_C99
903	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))	1197	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))
904	#else	1198	#else
905	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))	1199	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))
906	#endif	1200	#endif
907		1201
908	#if __cplusplus	1202	#if ECB_CPP
909	template<typename T>	1203	template<typename T>
910	static inline T ecb_div_rd (T val, T div)	1204	static inline T ecb_div_rd (T val, T div)
911	{	1205	{
912	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;	1206	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;
913	}	1207	}
…		…
930	}	1224	}
931	#else	1225	#else
932	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))	1226	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))
933	#endif	1227	#endif
934		1228
		1229	ecb_function_ ecb_const uint32_t ecb_binary16_to_binary32 (uint32_t x);
		1230	ecb_function_ ecb_const uint32_t
		1231	ecb_binary16_to_binary32 (uint32_t x)
		1232	{
		1233	unsigned int s = (x & 0x8000) << (31 - 15);
		1234	int e = (x >> 10) & 0x001f;
		1235	unsigned int m = x & 0x03ff;
		1236
		1237	if (ecb_expect_false (e == 31))
		1238	/* infinity or NaN */
		1239	e = 255 - (127 - 15);
		1240	else if (ecb_expect_false (!e))
		1241	{
		1242	if (ecb_expect_true (!m))
		1243	/* zero, handled by code below by forcing e to 0 */
		1244	e = 0 - (127 - 15);
		1245	else
		1246	{
		1247	/* subnormal, renormalise */
		1248	unsigned int s = 10 - ecb_ld32 (m);
		1249
		1250	m = (m << s) & 0x3ff; /* mask implicit bit */
		1251	e -= s - 1;
		1252	}
		1253	}
		1254
		1255	/* e and m now are normalised, or zero, (or inf or nan) */
		1256	e += 127 - 15;
		1257
		1258	return s | (e << 23) | (m << (23 - 10));
		1259	}
		1260
		1261	ecb_function_ ecb_const uint16_t ecb_binary32_to_binary16 (uint32_t x);
		1262	ecb_function_ ecb_const uint16_t
		1263	ecb_binary32_to_binary16 (uint32_t x)
		1264	{
		1265	unsigned int s = (x >> 16) & 0x00008000; /* sign bit, the easy part */
		1266	unsigned int e = ((x >> 23) & 0x000000ff) - (127 - 15); /* the desired exponent */
		1267	unsigned int m = x & 0x007fffff;
		1268
		1269	x &= 0x7fffffff;
		1270
		1271	/* if it's within range of binary16 normals, use fast path */
		1272	if (ecb_expect_true (0x38800000 <= x && x <= 0x477fefff))
		1273	{
		1274	/* mantissa round-to-even */
		1275	m += 0x00000fff + ((m >> (23 - 10)) & 1);
		1276
		1277	/* handle overflow */
		1278	if (ecb_expect_false (m >= 0x00800000))
		1279	{
		1280	m >>= 1;
		1281	e += 1;
		1282	}
		1283
		1284	return s | (e << 10) | (m >> (23 - 10));
		1285	}
		1286
		1287	/* handle large numbers and infinity */
		1288	if (ecb_expect_true (0x477fefff < x && x <= 0x7f800000))
		1289	return s | 0x7c00;
		1290
		1291	/* handle zero, subnormals and small numbers */
		1292	if (ecb_expect_true (x < 0x38800000))
		1293	{
		1294	/* zero */
		1295	if (ecb_expect_true (!x))
		1296	return s;
		1297
		1298	/* handle subnormals */
		1299
		1300	/* too small, will be zero */
		1301	if (e < (14 - 24)) /* might not be sharp, but is good enough */
		1302	return s;
		1303
		1304	m |= 0x00800000; /* make implicit bit explicit */
		1305
		1306	/* very tricky - we need to round to the nearest e (+10) bit value */
		1307	{
		1308	unsigned int bits = 14 - e;
		1309	unsigned int half = (1 << (bits - 1)) - 1;
		1310	unsigned int even = (m >> bits) & 1;
		1311
		1312	/* if this overflows, we will end up with a normalised number */
		1313	m = (m + half + even) >> bits;
		1314	}
		1315
		1316	return s | m;
		1317	}
		1318
		1319	/* handle NaNs, preserve leftmost nan bits, but make sure we don't turn them into infinities */
		1320	m >>= 13;
		1321
		1322	return s | 0x7c00 | m | !m;
		1323	}
		1324
		1325	/*******************************************************************************/
		1326	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */
		1327
		1328	/* basically, everything uses "ieee pure-endian" floating point numbers */
		1329	/* the only noteworthy exception is ancient armle, which uses order 43218765 */
		1330	#if 0 \
		1331	|| __i386 || __i386__ \
		1332	|| ECB_GCC_AMD64 \
		1333	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \
		1334	|| defined __s390__ || defined __s390x__ \
		1335	|| defined __mips__ \
		1336	|| defined __alpha__ \
		1337	|| defined __hppa__ \
		1338	|| defined __ia64__ \
		1339	|| defined __m68k__ \
		1340	|| defined __m88k__ \
		1341	|| defined __sh__ \
		1342	|| defined _M_IX86 || defined ECB_MSVC_AMD64 || defined _M_IA64 \
		1343	|| (defined __arm__ && (defined __ARM_EABI__ || defined __EABI__ || defined __VFP_FP__ || defined _WIN32_WCE || defined __ANDROID__)) \
		1344	|| defined __aarch64__
		1345	#define ECB_STDFP 1
		1346	#include <string.h> /* for memcpy */
		1347	#else
		1348	#define ECB_STDFP 0
		1349	#endif
		1350
		1351	#ifndef ECB_NO_LIBM
		1352
		1353	#include <math.h> /* for frexp*, ldexp*, INFINITY, NAN */
		1354
		1355	/* only the oldest of old doesn't have this one. solaris. */
		1356	#ifdef INFINITY
		1357	#define ECB_INFINITY INFINITY
		1358	#else
		1359	#define ECB_INFINITY HUGE_VAL
		1360	#endif
		1361
		1362	#ifdef NAN
		1363	#define ECB_NAN NAN
		1364	#else
		1365	#define ECB_NAN ECB_INFINITY
		1366	#endif
		1367
		1368	#if ECB_C99 || _XOPEN_VERSION >= 600 || _POSIX_VERSION >= 200112L
		1369	#define ecb_ldexpf(x,e) ldexpf ((x), (e))
		1370	#define ecb_frexpf(x,e) frexpf ((x), (e))
		1371	#else
		1372	#define ecb_ldexpf(x,e) (float) ldexp ((double) (x), (e))
		1373	#define ecb_frexpf(x,e) (float) frexp ((double) (x), (e))
		1374	#endif
		1375
		1376	/* convert a float to ieee single/binary32 */
		1377	ecb_function_ ecb_const uint32_t ecb_float_to_binary32 (float x);
		1378	ecb_function_ ecb_const uint32_t
		1379	ecb_float_to_binary32 (float x)
		1380	{
		1381	uint32_t r;
		1382
		1383	#if ECB_STDFP
		1384	memcpy (&r, &x, 4);
		1385	#else
		1386	/* slow emulation, works for anything but -0 */
		1387	uint32_t m;
		1388	int e;
		1389
		1390	if (x == 0e0f ) return 0x00000000U;
		1391	if (x > +3.40282346638528860e+38f) return 0x7f800000U;
		1392	if (x < -3.40282346638528860e+38f) return 0xff800000U;
		1393	if (x != x ) return 0x7fbfffffU;
		1394
		1395	m = ecb_frexpf (x, &e) * 0x1000000U;
		1396
		1397	r = m & 0x80000000U;
		1398
		1399	if (r)
		1400	m = -m;
		1401
		1402	if (e <= -126)
		1403	{
		1404	m &= 0xffffffU;
		1405	m >>= (-125 - e);
		1406	e = -126;
		1407	}
		1408
		1409	r |= (e + 126) << 23;
		1410	r |= m & 0x7fffffU;
		1411	#endif
		1412
		1413	return r;
		1414	}
		1415
		1416	/* converts an ieee single/binary32 to a float */
		1417	ecb_function_ ecb_const float ecb_binary32_to_float (uint32_t x);
		1418	ecb_function_ ecb_const float
		1419	ecb_binary32_to_float (uint32_t x)
		1420	{
		1421	float r;
		1422
		1423	#if ECB_STDFP
		1424	memcpy (&r, &x, 4);
		1425	#else
		1426	/* emulation, only works for normals and subnormals and +0 */
		1427	int neg = x >> 31;
		1428	int e = (x >> 23) & 0xffU;
		1429
		1430	x &= 0x7fffffU;
		1431
		1432	if (e)
		1433	x |= 0x800000U;
		1434	else
		1435	e = 1;
		1436
		1437	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */
		1438	r = ecb_ldexpf (x * (0.5f / 0x800000U), e - 126);
		1439
		1440	r = neg ? -r : r;
		1441	#endif
		1442
		1443	return r;
		1444	}
		1445
		1446	/* convert a double to ieee double/binary64 */
		1447	ecb_function_ ecb_const uint64_t ecb_double_to_binary64 (double x);
		1448	ecb_function_ ecb_const uint64_t
		1449	ecb_double_to_binary64 (double x)
		1450	{
		1451	uint64_t r;
		1452
		1453	#if ECB_STDFP
		1454	memcpy (&r, &x, 8);
		1455	#else
		1456	/* slow emulation, works for anything but -0 */
		1457	uint64_t m;
		1458	int e;
		1459
		1460	if (x == 0e0 ) return 0x0000000000000000U;
		1461	if (x > +1.79769313486231470e+308) return 0x7ff0000000000000U;
		1462	if (x < -1.79769313486231470e+308) return 0xfff0000000000000U;
		1463	if (x != x ) return 0X7ff7ffffffffffffU;
		1464
		1465	m = frexp (x, &e) * 0x20000000000000U;
		1466
		1467	r = m & 0x8000000000000000;;
		1468
		1469	if (r)
		1470	m = -m;
		1471
		1472	if (e <= -1022)
		1473	{
		1474	m &= 0x1fffffffffffffU;
		1475	m >>= (-1021 - e);
		1476	e = -1022;
		1477	}
		1478
		1479	r |= ((uint64_t)(e + 1022)) << 52;
		1480	r |= m & 0xfffffffffffffU;
		1481	#endif
		1482
		1483	return r;
		1484	}
		1485
		1486	/* converts an ieee double/binary64 to a double */
		1487	ecb_function_ ecb_const double ecb_binary64_to_double (uint64_t x);
		1488	ecb_function_ ecb_const double
		1489	ecb_binary64_to_double (uint64_t x)
		1490	{
		1491	double r;
		1492
		1493	#if ECB_STDFP
		1494	memcpy (&r, &x, 8);
		1495	#else
		1496	/* emulation, only works for normals and subnormals and +0 */
		1497	int neg = x >> 63;
		1498	int e = (x >> 52) & 0x7ffU;
		1499
		1500	x &= 0xfffffffffffffU;
		1501
		1502	if (e)
		1503	x |= 0x10000000000000U;
		1504	else
		1505	e = 1;
		1506
		1507	/* we distrust ldexp a bit and do the 2**-53 scaling by an extra multiply */
		1508	r = ldexp (x * (0.5 / 0x10000000000000U), e - 1022);
		1509
		1510	r = neg ? -r : r;
		1511	#endif
		1512
		1513	return r;
		1514	}
		1515
		1516	/* convert a float to ieee half/binary16 */
		1517	ecb_function_ ecb_const uint16_t ecb_float_to_binary16 (float x);
		1518	ecb_function_ ecb_const uint16_t
		1519	ecb_float_to_binary16 (float x)
		1520	{
		1521	return ecb_binary32_to_binary16 (ecb_float_to_binary32 (x));
		1522	}
		1523
		1524	/* convert an ieee half/binary16 to float */
		1525	ecb_function_ ecb_const float ecb_binary16_to_float (uint16_t x);
		1526	ecb_function_ ecb_const float
		1527	ecb_binary16_to_float (uint16_t x)
		1528	{
		1529	return ecb_binary32_to_float (ecb_binary16_to_binary32 (x));
		1530	}
		1531
		1532	#endif
		1533
935	#endif	1534	#endif
936		1535
937	/* ECB.H END */	1536	/* ECB.H END */
938		1537
939	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS	1538	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS
…		…
960	#define inline_size ecb_inline	1559	#define inline_size ecb_inline
961		1560
962	#if EV_FEATURE_CODE	1561	#if EV_FEATURE_CODE
963	# define inline_speed ecb_inline	1562	# define inline_speed ecb_inline
964	#else	1563	#else
965	# define inline_speed static noinline	1564	# define inline_speed noinline static
966	#endif	1565	#endif
967		1566
968	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)	1567	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)
969		1568
970	#if EV_MINPRI == EV_MAXPRI	1569	#if EV_MINPRI == EV_MAXPRI
971	# define ABSPRI(w) (((W)w), 0)	1570	# define ABSPRI(w) (((W)w), 0)
972	#else	1571	#else
973	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)	1572	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)
974	#endif	1573	#endif
975		1574
976	#define EMPTY /* required for microsofts broken pseudo-c compiler */	1575	#define EMPTY /* required for microsofts broken pseudo-c compiler */
977	#define EMPTY2(a,b) /* used to suppress some warnings */
978		1576
979	typedef ev_watcher *W;	1577	typedef ev_watcher *W;
980	typedef ev_watcher_list *WL;	1578	typedef ev_watcher_list *WL;
981	typedef ev_watcher_time *WT;	1579	typedef ev_watcher_time *WT;
982		1580
…		…
1007	# include "ev_win32.c"	1605	# include "ev_win32.c"
1008	#endif	1606	#endif
1009		1607
1010	/*****************************************************************************/	1608	/*****************************************************************************/
1011		1609
		1610	#if EV_USE_LINUXAIO
		1611	# include <linux/aio_abi.h> /* probably only needed for aio_context_t */
		1612	#endif
		1613
1012	/* define a suitable floor function (only used by periodics atm) */	1614	/* define a suitable floor function (only used by periodics atm) */
1013		1615
1014	#if EV_USE_FLOOR	1616	#if EV_USE_FLOOR
1015	# include <math.h>	1617	# include <math.h>
1016	# define ev_floor(v) floor (v)	1618	# define ev_floor(v) floor (v)
1017	#else	1619	#else
1018		1620
1019	#include <float.h>	1621	#include <float.h>
1020		1622
1021	/* a floor() replacement function, should be independent of ev_tstamp type */	1623	/* a floor() replacement function, should be independent of ev_tstamp type */
		1624	noinline
1022	static ev_tstamp noinline	1625	static ev_tstamp
1023	ev_floor (ev_tstamp v)	1626	ev_floor (ev_tstamp v)
1024	{	1627	{
1025	/* the choice of shift factor is not terribly important */	1628	/* the choice of shift factor is not terribly important */
1026	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */	1629	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */
1027	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;	1630	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;
…		…
1059		1662
1060	#ifdef __linux	1663	#ifdef __linux
1061	# include <sys/utsname.h>	1664	# include <sys/utsname.h>
1062	#endif	1665	#endif
1063		1666
1064	static unsigned int noinline ecb_cold	1667	noinline ecb_cold
		1668	static unsigned int
1065	ev_linux_version (void)	1669	ev_linux_version (void)
1066	{	1670	{
1067	#ifdef __linux	1671	#ifdef __linux
1068	unsigned int v = 0;	1672	unsigned int v = 0;
1069	struct utsname buf;	1673	struct utsname buf;
…		…
1098	}	1702	}
1099		1703
1100	/*****************************************************************************/	1704	/*****************************************************************************/
1101		1705
1102	#if EV_AVOID_STDIO	1706	#if EV_AVOID_STDIO
1103	static void noinline ecb_cold	1707	noinline ecb_cold
		1708	static void
1104	ev_printerr (const char *msg)	1709	ev_printerr (const char *msg)
1105	{	1710	{
1106	write (STDERR_FILENO, msg, strlen (msg));	1711	write (STDERR_FILENO, msg, strlen (msg));
1107	}	1712	}
1108	#endif	1713	#endif
1109		1714
1110	static void (*syserr_cb)(const char *msg) EV_THROW;	1715	static void (*syserr_cb)(const char *msg) EV_NOEXCEPT;
1111		1716
1112	void ecb_cold	1717	ecb_cold
		1718	void
1113	ev_set_syserr_cb (void (*cb)(const char *msg)) EV_THROW	1719	ev_set_syserr_cb (void (*cb)(const char *msg) EV_NOEXCEPT) EV_NOEXCEPT
1114	{	1720	{
1115	syserr_cb = cb;	1721	syserr_cb = cb;
1116	}	1722	}
1117		1723
1118	static void noinline ecb_cold	1724	noinline ecb_cold
		1725	static void
1119	ev_syserr (const char *msg)	1726	ev_syserr (const char *msg)
1120	{	1727	{
1121	if (!msg)	1728	if (!msg)
1122	msg = "(libev) system error";	1729	msg = "(libev) system error";
1123		1730
…		…
1136	abort ();	1743	abort ();
1137	}	1744	}
1138	}	1745	}
1139		1746
1140	static void *	1747	static void *
1141	ev_realloc_emul (void *ptr, long size)	1748	ev_realloc_emul (void *ptr, long size) EV_NOEXCEPT
1142	{	1749	{
1143	#if __GLIBC__
1144	return realloc (ptr, size);
1145	#else
1146	/* some systems, notably openbsd and darwin, fail to properly	1750	/* some systems, notably openbsd and darwin, fail to properly
1147	* implement realloc (x, 0) (as required by both ansi c-89 and	1751	* implement realloc (x, 0) (as required by both ansi c-89 and
1148	* the single unix specification, so work around them here.	1752	* the single unix specification, so work around them here.
		1753	* recently, also (at least) fedora and debian started breaking it,
		1754	* despite documenting it otherwise.
1149	*/	1755	*/
1150		1756
1151	if (size)	1757	if (size)
1152	return realloc (ptr, size);	1758	return realloc (ptr, size);
1153		1759
1154	free (ptr);	1760	free (ptr);
1155	return 0;	1761	return 0;
1156	#endif
1157	}	1762	}
1158		1763
1159	static void *(*alloc)(void *ptr, long size) EV_THROW = ev_realloc_emul;	1764	static void *(*alloc)(void *ptr, long size) EV_NOEXCEPT = ev_realloc_emul;
1160		1765
1161	void ecb_cold	1766	ecb_cold
		1767	void
1162	ev_set_allocator (void *(*cb)(void *ptr, long size)) EV_THROW	1768	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_NOEXCEPT) EV_NOEXCEPT
1163	{	1769	{
1164	alloc = cb;	1770	alloc = cb;
1165	}	1771	}
1166		1772
1167	inline_speed void *	1773	inline_speed void *
…		…
1194	typedef struct	1800	typedef struct
1195	{	1801	{
1196	WL head;	1802	WL head;
1197	unsigned char events; /* the events watched for */	1803	unsigned char events; /* the events watched for */
1198	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */	1804	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */
1199	unsigned char emask; /* the epoll backend stores the actual kernel mask in here */	1805	unsigned char emask; /* some backends store the actual kernel mask in here */
1200	unsigned char unused;	1806	unsigned char unused;
1201	#if EV_USE_EPOLL	1807	#if EV_USE_EPOLL
1202	unsigned int egen; /* generation counter to counter epoll bugs */	1808	unsigned int egen; /* generation counter to counter epoll bugs */
1203	#endif	1809	#endif
1204	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP	1810	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP
…		…
1284		1890
1285	/*****************************************************************************/	1891	/*****************************************************************************/
1286		1892
1287	#ifndef EV_HAVE_EV_TIME	1893	#ifndef EV_HAVE_EV_TIME
1288	ev_tstamp	1894	ev_tstamp
1289	ev_time (void) EV_THROW	1895	ev_time (void) EV_NOEXCEPT
1290	{	1896	{
1291	#if EV_USE_REALTIME	1897	#if EV_USE_REALTIME
1292	if (expect_true (have_realtime))	1898	if (expect_true (have_realtime))
1293	{	1899	{
1294	struct timespec ts;	1900	struct timespec ts;
…		…
1318	return ev_time ();	1924	return ev_time ();
1319	}	1925	}
1320		1926
1321	#if EV_MULTIPLICITY	1927	#if EV_MULTIPLICITY
1322	ev_tstamp	1928	ev_tstamp
1323	ev_now (EV_P) EV_THROW	1929	ev_now (EV_P) EV_NOEXCEPT
1324	{	1930	{
1325	return ev_rt_now;	1931	return ev_rt_now;
1326	}	1932	}
1327	#endif	1933	#endif
1328		1934
1329	void	1935	void
1330	ev_sleep (ev_tstamp delay) EV_THROW	1936	ev_sleep (ev_tstamp delay) EV_NOEXCEPT
1331	{	1937	{
1332	if (delay > 0.)	1938	if (delay > 0.)
1333	{	1939	{
1334	#if EV_USE_NANOSLEEP	1940	#if EV_USE_NANOSLEEP
1335	struct timespec ts;	1941	struct timespec ts;
1336		1942
1337	EV_TS_SET (ts, delay);	1943	EV_TS_SET (ts, delay);
1338	nanosleep (&ts, 0);	1944	nanosleep (&ts, 0);
1339	#elif defined _WIN32	1945	#elif defined _WIN32
		1946	/* maybe this should round up, as ms is very low resolution */
		1947	/* compared to select (µs) or nanosleep (ns) */
1340	Sleep ((unsigned long)(delay * 1e3));	1948	Sleep ((unsigned long)(delay * 1e3));
1341	#else	1949	#else
1342	struct timeval tv;	1950	struct timeval tv;
1343		1951
1344	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */	1952	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */
…		…
1375	}	1983	}
1376		1984
1377	return ncur;	1985	return ncur;
1378	}	1986	}
1379		1987
1380	static void * noinline ecb_cold	1988	noinline ecb_cold
		1989	static void *
1381	array_realloc (int elem, void *base, int *cur, int cnt)	1990	array_realloc (int elem, void *base, int *cur, int cnt)
1382	{	1991	{
1383	*cur = array_nextsize (elem, *cur, cnt);	1992	*cur = array_nextsize (elem, *cur, cnt);
1384	return ev_realloc (base, elem * *cur);	1993	return ev_realloc (base, elem * *cur);
1385	}	1994	}
1386		1995
		1996	#define array_needsize_noinit(base,offset,count)
		1997
1387	#define array_init_zero(base,count) \	1998	#define array_needsize_zerofill(base,offset,count) \
1388	memset ((void *)(base), 0, sizeof (*(base)) * (count))	1999	memset ((void *)(base + offset), 0, sizeof (*(base)) * (count))
1389		2000
1390	#define array_needsize(type,base,cur,cnt,init) \	2001	#define array_needsize(type,base,cur,cnt,init) \
1391	if (expect_false ((cnt) > (cur))) \	2002	if (expect_false ((cnt) > (cur))) \
1392	{ \	2003	{ \
1393	int ecb_unused ocur_ = (cur); \	2004	ecb_unused int ocur_ = (cur); \
1394	(base) = (type *)array_realloc \	2005	(base) = (type *)array_realloc \
1395	(sizeof (type), (base), &(cur), (cnt)); \	2006	(sizeof (type), (base), &(cur), (cnt)); \
1396	init ((base) + (ocur_), (cur) - ocur_); \	2007	init ((base), ocur_, ((cur) - ocur_)); \
1397	}	2008	}
1398		2009
1399	#if 0	2010	#if 0
1400	#define array_slim(type,stem) \	2011	#define array_slim(type,stem) \
1401	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \	2012	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \
…		…
1410	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0	2021	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0
1411		2022
1412	/*****************************************************************************/	2023	/*****************************************************************************/
1413		2024
1414	/* dummy callback for pending events */	2025	/* dummy callback for pending events */
1415	static void noinline	2026	noinline
		2027	static void
1416	pendingcb (EV_P_ ev_prepare *w, int revents)	2028	pendingcb (EV_P_ ev_prepare *w, int revents)
1417	{	2029	{
1418	}	2030	}
1419		2031
1420	void noinline	2032	noinline
		2033	void
1421	ev_feed_event (EV_P_ void *w, int revents) EV_THROW	2034	ev_feed_event (EV_P_ void *w, int revents) EV_NOEXCEPT
1422	{	2035	{
1423	W w_ = (W)w;	2036	W w_ = (W)w;
1424	int pri = ABSPRI (w_);	2037	int pri = ABSPRI (w_);
1425		2038
1426	if (expect_false (w_->pending))	2039	if (expect_false (w_->pending))
1427	pendings [pri][w_->pending - 1].events |= revents;	2040	pendings [pri][w_->pending - 1].events |= revents;
1428	else	2041	else
1429	{	2042	{
1430	w_->pending = ++pendingcnt [pri];	2043	w_->pending = ++pendingcnt [pri];
1431	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, EMPTY2);	2044	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, array_needsize_noinit);
1432	pendings [pri][w_->pending - 1].w = w_;	2045	pendings [pri][w_->pending - 1].w = w_;
1433	pendings [pri][w_->pending - 1].events = revents;	2046	pendings [pri][w_->pending - 1].events = revents;
1434	}	2047	}
1435		2048
1436	pendingpri = NUMPRI - 1;	2049	pendingpri = NUMPRI - 1;
1437	}	2050	}
1438		2051
1439	inline_speed void	2052	inline_speed void
1440	feed_reverse (EV_P_ W w)	2053	feed_reverse (EV_P_ W w)
1441	{	2054	{
1442	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, EMPTY2);	2055	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, array_needsize_noinit);
1443	rfeeds [rfeedcnt++] = w;	2056	rfeeds [rfeedcnt++] = w;
1444	}	2057	}
1445		2058
1446	inline_size void	2059	inline_size void
1447	feed_reverse_done (EV_P_ int revents)	2060	feed_reverse_done (EV_P_ int revents)
…		…
1487	if (expect_true (!anfd->reify))	2100	if (expect_true (!anfd->reify))
1488	fd_event_nocheck (EV_A_ fd, revents);	2101	fd_event_nocheck (EV_A_ fd, revents);
1489	}	2102	}
1490		2103
1491	void	2104	void
1492	ev_feed_fd_event (EV_P_ int fd, int revents) EV_THROW	2105	ev_feed_fd_event (EV_P_ int fd, int revents) EV_NOEXCEPT
1493	{	2106	{
1494	if (fd >= 0 && fd < anfdmax)	2107	if (fd >= 0 && fd < anfdmax)
1495	fd_event_nocheck (EV_A_ fd, revents);	2108	fd_event_nocheck (EV_A_ fd, revents);
1496	}	2109	}
1497		2110
…		…
1534	ev_io *w;	2147	ev_io *w;
1535		2148
1536	unsigned char o_events = anfd->events;	2149	unsigned char o_events = anfd->events;
1537	unsigned char o_reify = anfd->reify;	2150	unsigned char o_reify = anfd->reify;
1538		2151
1539	anfd->reify = 0;	2152	anfd->reify = 0;
1540		2153
1541	/*if (expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */	2154	/*if (expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */
1542	{	2155	{
1543	anfd->events = 0;	2156	anfd->events = 0;
1544		2157
…		…
1555		2168
1556	fdchangecnt = 0;	2169	fdchangecnt = 0;
1557	}	2170	}
1558		2171
1559	/* something about the given fd changed */	2172	/* something about the given fd changed */
1560	inline_size void	2173	inline_size
		2174	void
1561	fd_change (EV_P_ int fd, int flags)	2175	fd_change (EV_P_ int fd, int flags)
1562	{	2176	{
1563	unsigned char reify = anfds [fd].reify;	2177	unsigned char reify = anfds [fd].reify;
1564	anfds [fd].reify |= flags;	2178	anfds [fd].reify |= flags;
1565		2179
1566	if (expect_true (!reify))	2180	if (expect_true (!reify))
1567	{	2181	{
1568	++fdchangecnt;	2182	++fdchangecnt;
1569	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, EMPTY2);	2183	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, array_needsize_noinit);
1570	fdchanges [fdchangecnt - 1] = fd;	2184	fdchanges [fdchangecnt - 1] = fd;
1571	}	2185	}
1572	}	2186	}
1573		2187
1574	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */	2188	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */
1575	inline_speed void ecb_cold	2189	inline_speed ecb_cold void
1576	fd_kill (EV_P_ int fd)	2190	fd_kill (EV_P_ int fd)
1577	{	2191	{
1578	ev_io *w;	2192	ev_io *w;
1579		2193
1580	while ((w = (ev_io *)anfds [fd].head))	2194	while ((w = (ev_io *)anfds [fd].head))
…		…
1583	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);	2197	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);
1584	}	2198	}
1585	}	2199	}
1586		2200
1587	/* check whether the given fd is actually valid, for error recovery */	2201	/* check whether the given fd is actually valid, for error recovery */
1588	inline_size int ecb_cold	2202	inline_size ecb_cold int
1589	fd_valid (int fd)	2203	fd_valid (int fd)
1590	{	2204	{
1591	#ifdef _WIN32	2205	#ifdef _WIN32
1592	return EV_FD_TO_WIN32_HANDLE (fd) != -1;	2206	return EV_FD_TO_WIN32_HANDLE (fd) != -1;
1593	#else	2207	#else
1594	return fcntl (fd, F_GETFD) != -1;	2208	return fcntl (fd, F_GETFD) != -1;
1595	#endif	2209	#endif
1596	}	2210	}
1597		2211
1598	/* called on EBADF to verify fds */	2212	/* called on EBADF to verify fds */
1599	static void noinline ecb_cold	2213	noinline ecb_cold
		2214	static void
1600	fd_ebadf (EV_P)	2215	fd_ebadf (EV_P)
1601	{	2216	{
1602	int fd;	2217	int fd;
1603		2218
1604	for (fd = 0; fd < anfdmax; ++fd)	2219	for (fd = 0; fd < anfdmax; ++fd)
…		…
1606	if (!fd_valid (fd) && errno == EBADF)	2221	if (!fd_valid (fd) && errno == EBADF)
1607	fd_kill (EV_A_ fd);	2222	fd_kill (EV_A_ fd);
1608	}	2223	}
1609		2224
1610	/* called on ENOMEM in select/poll to kill some fds and retry */	2225	/* called on ENOMEM in select/poll to kill some fds and retry */
1611	static void noinline ecb_cold	2226	noinline ecb_cold
		2227	static void
1612	fd_enomem (EV_P)	2228	fd_enomem (EV_P)
1613	{	2229	{
1614	int fd;	2230	int fd;
1615		2231
1616	for (fd = anfdmax; fd--; )	2232	for (fd = anfdmax; fd--; )
…		…
1620	break;	2236	break;
1621	}	2237	}
1622	}	2238	}
1623		2239
1624	/* usually called after fork if backend needs to re-arm all fds from scratch */	2240	/* usually called after fork if backend needs to re-arm all fds from scratch */
1625	static void noinline	2241	noinline
		2242	static void
1626	fd_rearm_all (EV_P)	2243	fd_rearm_all (EV_P)
1627	{	2244	{
1628	int fd;	2245	int fd;
1629		2246
1630	for (fd = 0; fd < anfdmax; ++fd)	2247	for (fd = 0; fd < anfdmax; ++fd)
…		…
1811		2428
1812	/*****************************************************************************/	2429	/*****************************************************************************/
1813		2430
1814	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	2431	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
1815		2432
1816	static void noinline ecb_cold	2433	noinline ecb_cold
		2434	static void
1817	evpipe_init (EV_P)	2435	evpipe_init (EV_P)
1818	{	2436	{
1819	if (!ev_is_active (&pipe_w))	2437	if (!ev_is_active (&pipe_w))
1820	{	2438	{
		2439	int fds [2];
		2440
1821	# if EV_USE_EVENTFD	2441	# if EV_USE_EVENTFD
		2442	fds [0] = -1;
1822	evfd = eventfd (0, EFD_NONBLOCK | EFD_CLOEXEC);	2443	fds [1] = eventfd (0, EFD_NONBLOCK | EFD_CLOEXEC);
1823	if (evfd < 0 && errno == EINVAL)	2444	if (fds [1] < 0 && errno == EINVAL)
1824	evfd = eventfd (0, 0);	2445	fds [1] = eventfd (0, 0);
1825		2446
1826	if (evfd >= 0)	2447	if (fds [1] < 0)
		2448	# endif
1827	{	2449	{
		2450	while (pipe (fds))
		2451	ev_syserr ("(libev) error creating signal/async pipe");
		2452
		2453	fd_intern (fds [0]);
		2454	}
		2455
1828	evpipe [0] = -1;	2456	evpipe [0] = fds [0];
1829	fd_intern (evfd); /* doing it twice doesn't hurt */	2457
1830	ev_io_set (&pipe_w, evfd, EV_READ);	2458	if (evpipe [1] < 0)
		2459	evpipe [1] = fds [1]; /* first call, set write fd */
		2460	else
		2461	{
		2462	/* on subsequent calls, do not change evpipe [1] */
		2463	/* so that evpipe_write can always rely on its value. */
		2464	/* this branch does not do anything sensible on windows, */
		2465	/* so must not be executed on windows */
		2466
		2467	dup2 (fds [1], evpipe [1]);
		2468	close (fds [1]);
		2469	}
		2470
		2471	fd_intern (evpipe [1]);
		2472
		2473	ev_io_set (&pipe_w, evpipe [0] < 0 ? evpipe [1] : evpipe [0], EV_READ);
		2474	ev_io_start (EV_A_ &pipe_w);
		2475	ev_unref (EV_A); /* watcher should not keep loop alive */
		2476	}
		2477	}
		2478
		2479	inline_speed void
		2480	evpipe_write (EV_P_ EV_ATOMIC_T *flag)
		2481	{
		2482	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */
		2483
		2484	if (expect_true (*flag))
		2485	return;
		2486
		2487	*flag = 1;
		2488	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */
		2489
		2490	pipe_write_skipped = 1;
		2491
		2492	ECB_MEMORY_FENCE; /* make sure pipe_write_skipped is visible before we check pipe_write_wanted */
		2493
		2494	if (pipe_write_wanted)
		2495	{
		2496	int old_errno;
		2497
		2498	pipe_write_skipped = 0;
		2499	ECB_MEMORY_FENCE_RELEASE;
		2500
		2501	old_errno = errno; /* save errno because write will clobber it */
		2502
		2503	#if EV_USE_EVENTFD
		2504	if (evpipe [0] < 0)
		2505	{
		2506	uint64_t counter = 1;
		2507	write (evpipe [1], &counter, sizeof (uint64_t));
1831	}	2508	}
1832	else	2509	else
1833	# endif	2510	#endif
1834	{	2511	{
1835	while (pipe (evpipe))	2512	#ifdef _WIN32
1836	ev_syserr ("(libev) error creating signal/async pipe");	2513	WSABUF buf;
1837		2514	DWORD sent;
1838	fd_intern (evpipe [0]);	2515	buf.buf = (char *)&buf;
1839	fd_intern (evpipe [1]);	2516	buf.len = 1;
1840	ev_io_set (&pipe_w, evpipe [0], EV_READ);	2517	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);
1841	}	2518	#else
1842
1843	ev_io_start (EV_A_ &pipe_w);
1844	ev_unref (EV_A); /* watcher should not keep loop alive */
1845	}
1846	}
1847
1848	inline_speed void
1849	evpipe_write (EV_P_ EV_ATOMIC_T *flag)
1850	{
1851	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */
1852
1853	if (expect_true (*flag))
1854	return;
1855
1856	*flag = 1;
1857
1858	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */
1859
1860	pipe_write_skipped = 1;
1861
1862	ECB_MEMORY_FENCE; /* make sure pipe_write_skipped is visible before we check pipe_write_wanted */
1863
1864	if (pipe_write_wanted)
1865	{
1866	int old_errno;
1867
1868	pipe_write_skipped = 0; /* just an optimisation, no fence needed */
1869
1870	old_errno = errno; /* save errno because write will clobber it */
1871
1872	#if EV_USE_EVENTFD
1873	if (evfd >= 0)
1874	{
1875	uint64_t counter = 1;
1876	write (evfd, &counter, sizeof (uint64_t));
1877	}
1878	else
1879	#endif
1880	{
1881	/* win32 people keep sending patches that change this write() to send() */
1882	/* and then run away. but send() is wrong, it wants a socket handle on win32 */
1883	/* so when you think this write should be a send instead, please find out */
1884	/* where your send() is from - it's definitely not the microsoft send, and */
1885	/* tell me. thank you. */
1886	/* it might be that your problem is that your environment needs EV_USE_WSASOCKET */
1887	/* check the ev documentation on how to use this flag */
1888	write (evpipe [1], &(evpipe [1]), 1);	2519	write (evpipe [1], &(evpipe [1]), 1);
		2520	#endif
1889	}	2521	}
1890		2522
1891	errno = old_errno;	2523	errno = old_errno;
1892	}	2524	}
1893	}	2525	}
…		…
1900	int i;	2532	int i;
1901		2533
1902	if (revents & EV_READ)	2534	if (revents & EV_READ)
1903	{	2535	{
1904	#if EV_USE_EVENTFD	2536	#if EV_USE_EVENTFD
1905	if (evfd >= 0)	2537	if (evpipe [0] < 0)
1906	{	2538	{
1907	uint64_t counter;	2539	uint64_t counter;
1908	read (evfd, &counter, sizeof (uint64_t));	2540	read (evpipe [1], &counter, sizeof (uint64_t));
1909	}	2541	}
1910	else	2542	else
1911	#endif	2543	#endif
1912	{	2544	{
1913	char dummy;	2545	char dummy[4];
1914	/* see discussion in evpipe_write when you think this read should be recv in win32 */	2546	#ifdef _WIN32
		2547	WSABUF buf;
		2548	DWORD recvd;
		2549	DWORD flags = 0;
		2550	buf.buf = dummy;
		2551	buf.len = sizeof (dummy);
		2552	WSARecv (EV_FD_TO_WIN32_HANDLE (evpipe [0]), &buf, 1, &recvd, &flags, 0, 0);
		2553	#else
1915	read (evpipe [0], &dummy, 1);	2554	read (evpipe [0], &dummy, sizeof (dummy));
		2555	#endif
1916	}	2556	}
1917	}	2557	}
1918		2558
1919	pipe_write_skipped = 0;	2559	pipe_write_skipped = 0;
1920		2560
…		…
1923	#if EV_SIGNAL_ENABLE	2563	#if EV_SIGNAL_ENABLE
1924	if (sig_pending)	2564	if (sig_pending)
1925	{	2565	{
1926	sig_pending = 0;	2566	sig_pending = 0;
1927		2567
1928	ECB_MEMORY_FENCE_RELEASE;	2568	ECB_MEMORY_FENCE;
1929		2569
1930	for (i = EV_NSIG - 1; i--; )	2570	for (i = EV_NSIG - 1; i--; )
1931	if (expect_false (signals [i].pending))	2571	if (expect_false (signals [i].pending))
1932	ev_feed_signal_event (EV_A_ i + 1);	2572	ev_feed_signal_event (EV_A_ i + 1);
1933	}	2573	}
…		…
1936	#if EV_ASYNC_ENABLE	2576	#if EV_ASYNC_ENABLE
1937	if (async_pending)	2577	if (async_pending)
1938	{	2578	{
1939	async_pending = 0;	2579	async_pending = 0;
1940		2580
1941	ECB_MEMORY_FENCE_RELEASE;	2581	ECB_MEMORY_FENCE;
1942		2582
1943	for (i = asynccnt; i--; )	2583	for (i = asynccnt; i--; )
1944	if (asyncs [i]->sent)	2584	if (asyncs [i]->sent)
1945	{	2585	{
1946	asyncs [i]->sent = 0;	2586	asyncs [i]->sent = 0;
		2587	ECB_MEMORY_FENCE_RELEASE;
1947	ev_feed_event (EV_A_ asyncs [i], EV_ASYNC);	2588	ev_feed_event (EV_A_ asyncs [i], EV_ASYNC);
1948	}	2589	}
1949	}	2590	}
1950	#endif	2591	#endif
1951	}	2592	}
1952		2593
1953	/*****************************************************************************/	2594	/*****************************************************************************/
1954		2595
1955	void	2596	void
1956	ev_feed_signal (int signum) EV_THROW	2597	ev_feed_signal (int signum) EV_NOEXCEPT
1957	{	2598	{
1958	#if EV_MULTIPLICITY	2599	#if EV_MULTIPLICITY
		2600	EV_P;
		2601	ECB_MEMORY_FENCE_ACQUIRE;
1959	EV_P = signals [signum - 1].loop;	2602	EV_A = signals [signum - 1].loop;
1960		2603
1961	if (!EV_A)	2604	if (!EV_A)
1962	return;	2605	return;
1963	#endif	2606	#endif
1964		2607
1965	if (!ev_active (&pipe_w))
1966	return;
1967
1968	signals [signum - 1].pending = 1;	2608	signals [signum - 1].pending = 1;
1969	evpipe_write (EV_A_ &sig_pending);	2609	evpipe_write (EV_A_ &sig_pending);
1970	}	2610	}
1971		2611
1972	static void	2612	static void
…		…
1977	#endif	2617	#endif
1978		2618
1979	ev_feed_signal (signum);	2619	ev_feed_signal (signum);
1980	}	2620	}
1981		2621
1982	void noinline	2622	noinline
		2623	void
1983	ev_feed_signal_event (EV_P_ int signum) EV_THROW	2624	ev_feed_signal_event (EV_P_ int signum) EV_NOEXCEPT
1984	{	2625	{
1985	WL w;	2626	WL w;
1986		2627
1987	if (expect_false (signum <= 0 || signum > EV_NSIG))	2628	if (expect_false (signum <= 0 || signum >= EV_NSIG))
1988	return;	2629	return;
1989		2630
1990	--signum;	2631	--signum;
1991		2632
1992	#if EV_MULTIPLICITY	2633	#if EV_MULTIPLICITY
…		…
1996	if (expect_false (signals [signum].loop != EV_A))	2637	if (expect_false (signals [signum].loop != EV_A))
1997	return;	2638	return;
1998	#endif	2639	#endif
1999		2640
2000	signals [signum].pending = 0;	2641	signals [signum].pending = 0;
		2642	ECB_MEMORY_FENCE_RELEASE;
2001		2643
2002	for (w = signals [signum].head; w; w = w->next)	2644	for (w = signals [signum].head; w; w = w->next)
2003	ev_feed_event (EV_A_ (W)w, EV_SIGNAL);	2645	ev_feed_event (EV_A_ (W)w, EV_SIGNAL);
2004	}	2646	}
2005		2647
…		…
2096	# include "ev_kqueue.c"	2738	# include "ev_kqueue.c"
2097	#endif	2739	#endif
2098	#if EV_USE_EPOLL	2740	#if EV_USE_EPOLL
2099	# include "ev_epoll.c"	2741	# include "ev_epoll.c"
2100	#endif	2742	#endif
		2743	#if EV_USE_LINUXAIO
		2744	# include "ev_linuxaio.c"
		2745	#endif
2101	#if EV_USE_POLL	2746	#if EV_USE_POLL
2102	# include "ev_poll.c"	2747	# include "ev_poll.c"
2103	#endif	2748	#endif
2104	#if EV_USE_SELECT	2749	#if EV_USE_SELECT
2105	# include "ev_select.c"	2750	# include "ev_select.c"
2106	#endif	2751	#endif
2107		2752
2108	int ecb_cold	2753	ecb_cold int
2109	ev_version_major (void) EV_THROW	2754	ev_version_major (void) EV_NOEXCEPT
2110	{	2755	{
2111	return EV_VERSION_MAJOR;	2756	return EV_VERSION_MAJOR;
2112	}	2757	}
2113		2758
2114	int ecb_cold	2759	ecb_cold int
2115	ev_version_minor (void) EV_THROW	2760	ev_version_minor (void) EV_NOEXCEPT
2116	{	2761	{
2117	return EV_VERSION_MINOR;	2762	return EV_VERSION_MINOR;
2118	}	2763	}
2119		2764
2120	/* return true if we are running with elevated privileges and should ignore env variables */	2765	/* return true if we are running with elevated privileges and should ignore env variables */
2121	int inline_size ecb_cold	2766	inline_size ecb_cold int
2122	enable_secure (void)	2767	enable_secure (void)
2123	{	2768	{
2124	#ifdef _WIN32	2769	#ifdef _WIN32
2125	return 0;	2770	return 0;
2126	#else	2771	#else
2127	return getuid () != geteuid ()	2772	return getuid () != geteuid ()
2128	|| getgid () != getegid ();	2773	|| getgid () != getegid ();
2129	#endif	2774	#endif
2130	}	2775	}
2131		2776
2132	unsigned int ecb_cold	2777	ecb_cold
		2778	unsigned int
2133	ev_supported_backends (void) EV_THROW	2779	ev_supported_backends (void) EV_NOEXCEPT
2134	{	2780	{
2135	unsigned int flags = 0;	2781	unsigned int flags = 0;
2136		2782
2137	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;	2783	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;
2138	if (EV_USE_KQUEUE) flags |= EVBACKEND_KQUEUE;	2784	if (EV_USE_KQUEUE ) flags |= EVBACKEND_KQUEUE;
2139	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;	2785	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;
		2786	if (EV_USE_LINUXAIO) flags |= EVBACKEND_LINUXAIO;
2140	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;	2787	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;
2141	if (EV_USE_SELECT) flags |= EVBACKEND_SELECT;	2788	if (EV_USE_SELECT ) flags |= EVBACKEND_SELECT;
2142		2789
2143	return flags;	2790	return flags;
2144	}	2791	}
2145		2792
2146	unsigned int ecb_cold	2793	ecb_cold
		2794	unsigned int
2147	ev_recommended_backends (void) EV_THROW	2795	ev_recommended_backends (void) EV_NOEXCEPT
2148	{	2796	{
2149	unsigned int flags = ev_supported_backends ();	2797	unsigned int flags = ev_supported_backends ();
2150		2798
2151	#ifndef __NetBSD__	2799	#ifndef __NetBSD__
2152	/* kqueue is borked on everything but netbsd apparently */	2800	/* kqueue is borked on everything but netbsd apparently */
…		…
2160	#endif	2808	#endif
2161	#ifdef __FreeBSD__	2809	#ifdef __FreeBSD__
2162	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */	2810	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */
2163	#endif	2811	#endif
2164		2812
		2813	/* TODO: linuxaio is very experimental */
		2814	#if !EV_RECOMMEND_LINUXAIO
		2815	flags &= ~EVBACKEND_LINUXAIO;
		2816	#endif
		2817
2165	return flags;	2818	return flags;
2166	}	2819	}
2167		2820
2168	unsigned int ecb_cold	2821	ecb_cold
		2822	unsigned int
2169	ev_embeddable_backends (void) EV_THROW	2823	ev_embeddable_backends (void) EV_NOEXCEPT
2170	{	2824	{
2171	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;	2825	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;
2172		2826
2173	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */	2827	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */
2174	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */	2828	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */
…		…
2176		2830
2177	return flags;	2831	return flags;
2178	}	2832	}
2179		2833
2180	unsigned int	2834	unsigned int
2181	ev_backend (EV_P) EV_THROW	2835	ev_backend (EV_P) EV_NOEXCEPT
2182	{	2836	{
2183	return backend;	2837	return backend;
2184	}	2838	}
2185		2839
2186	#if EV_FEATURE_API	2840	#if EV_FEATURE_API
2187	unsigned int	2841	unsigned int
2188	ev_iteration (EV_P) EV_THROW	2842	ev_iteration (EV_P) EV_NOEXCEPT
2189	{	2843	{
2190	return loop_count;	2844	return loop_count;
2191	}	2845	}
2192		2846
2193	unsigned int	2847	unsigned int
2194	ev_depth (EV_P) EV_THROW	2848	ev_depth (EV_P) EV_NOEXCEPT
2195	{	2849	{
2196	return loop_depth;	2850	return loop_depth;
2197	}	2851	}
2198		2852
2199	void	2853	void
2200	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2854	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2201	{	2855	{
2202	io_blocktime = interval;	2856	io_blocktime = interval;
2203	}	2857	}
2204		2858
2205	void	2859	void
2206	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2860	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2207	{	2861	{
2208	timeout_blocktime = interval;	2862	timeout_blocktime = interval;
2209	}	2863	}
2210		2864
2211	void	2865	void
2212	ev_set_userdata (EV_P_ void *data) EV_THROW	2866	ev_set_userdata (EV_P_ void *data) EV_NOEXCEPT
2213	{	2867	{
2214	userdata = data;	2868	userdata = data;
2215	}	2869	}
2216		2870
2217	void *	2871	void *
2218	ev_userdata (EV_P) EV_THROW	2872	ev_userdata (EV_P) EV_NOEXCEPT
2219	{	2873	{
2220	return userdata;	2874	return userdata;
2221	}	2875	}
2222		2876
2223	void	2877	void
2224	ev_set_invoke_pending_cb (EV_P_ void (*invoke_pending_cb)(EV_P)) EV_THROW	2878	ev_set_invoke_pending_cb (EV_P_ ev_loop_callback invoke_pending_cb) EV_NOEXCEPT
2225	{	2879	{
2226	invoke_cb = invoke_pending_cb;	2880	invoke_cb = invoke_pending_cb;
2227	}	2881	}
2228		2882
2229	void	2883	void
2230	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_THROW, void (*acquire)(EV_P) EV_THROW) EV_THROW	2884	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_NOEXCEPT, void (*acquire)(EV_P) EV_NOEXCEPT) EV_NOEXCEPT
2231	{	2885	{
2232	release_cb = release;	2886	release_cb = release;
2233	acquire_cb = acquire;	2887	acquire_cb = acquire;
2234	}	2888	}
2235	#endif	2889	#endif
2236		2890
2237	/* initialise a loop structure, must be zero-initialised */	2891	/* initialise a loop structure, must be zero-initialised */
2238	static void noinline ecb_cold	2892	noinline ecb_cold
		2893	static void
2239	loop_init (EV_P_ unsigned int flags) EV_THROW	2894	loop_init (EV_P_ unsigned int flags) EV_NOEXCEPT
2240	{	2895	{
2241	if (!backend)	2896	if (!backend)
2242	{	2897	{
2243	origflags = flags;	2898	origflags = flags;
2244		2899
…		…
2289	#if EV_ASYNC_ENABLE	2944	#if EV_ASYNC_ENABLE
2290	async_pending = 0;	2945	async_pending = 0;
2291	#endif	2946	#endif
2292	pipe_write_skipped = 0;	2947	pipe_write_skipped = 0;
2293	pipe_write_wanted = 0;	2948	pipe_write_wanted = 0;
		2949	evpipe [0] = -1;
		2950	evpipe [1] = -1;
2294	#if EV_USE_INOTIFY	2951	#if EV_USE_INOTIFY
2295	fs_fd = flags & EVFLAG_NOINOTIFY ? -1 : -2;	2952	fs_fd = flags & EVFLAG_NOINOTIFY ? -1 : -2;
2296	#endif	2953	#endif
2297	#if EV_USE_SIGNALFD	2954	#if EV_USE_SIGNALFD
2298	sigfd = flags & EVFLAG_SIGNALFD ? -2 : -1;	2955	sigfd = flags & EVFLAG_SIGNALFD ? -2 : -1;
…		…
2300		2957
2301	if (!(flags & EVBACKEND_MASK))	2958	if (!(flags & EVBACKEND_MASK))
2302	flags |= ev_recommended_backends ();	2959	flags |= ev_recommended_backends ();
2303		2960
2304	#if EV_USE_IOCP	2961	#if EV_USE_IOCP
2305	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);	2962	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);
2306	#endif	2963	#endif
2307	#if EV_USE_PORT	2964	#if EV_USE_PORT
2308	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);	2965	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);
2309	#endif	2966	#endif
2310	#if EV_USE_KQUEUE	2967	#if EV_USE_KQUEUE
2311	if (!backend && (flags & EVBACKEND_KQUEUE)) backend = kqueue_init (EV_A_ flags);	2968	if (!backend && (flags & EVBACKEND_KQUEUE )) backend = kqueue_init (EV_A_ flags);
		2969	#endif
		2970	#if EV_USE_LINUXAIO
		2971	if (!backend && (flags & EVBACKEND_LINUXAIO)) backend = linuxaio_init (EV_A_ flags);
2312	#endif	2972	#endif
2313	#if EV_USE_EPOLL	2973	#if EV_USE_EPOLL
2314	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);	2974	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);
2315	#endif	2975	#endif
2316	#if EV_USE_POLL	2976	#if EV_USE_POLL
2317	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);	2977	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);
2318	#endif	2978	#endif
2319	#if EV_USE_SELECT	2979	#if EV_USE_SELECT
2320	if (!backend && (flags & EVBACKEND_SELECT)) backend = select_init (EV_A_ flags);	2980	if (!backend && (flags & EVBACKEND_SELECT )) backend = select_init (EV_A_ flags);
2321	#endif	2981	#endif
2322		2982
2323	ev_prepare_init (&pending_w, pendingcb);	2983	ev_prepare_init (&pending_w, pendingcb);
2324		2984
2325	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	2985	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
…		…
2328	#endif	2988	#endif
2329	}	2989	}
2330	}	2990	}
2331		2991
2332	/* free up a loop structure */	2992	/* free up a loop structure */
2333	void ecb_cold	2993	ecb_cold
		2994	void
2334	ev_loop_destroy (EV_P)	2995	ev_loop_destroy (EV_P)
2335	{	2996	{
2336	int i;	2997	int i;
2337		2998
2338	#if EV_MULTIPLICITY	2999	#if EV_MULTIPLICITY
…		…
2349	EV_INVOKE_PENDING;	3010	EV_INVOKE_PENDING;
2350	}	3011	}
2351	#endif	3012	#endif
2352		3013
2353	#if EV_CHILD_ENABLE	3014	#if EV_CHILD_ENABLE
2354	if (ev_is_active (&childev))	3015	if (ev_is_default_loop (EV_A) && ev_is_active (&childev))
2355	{	3016	{
2356	ev_ref (EV_A); /* child watcher */	3017	ev_ref (EV_A); /* child watcher */
2357	ev_signal_stop (EV_A_ &childev);	3018	ev_signal_stop (EV_A_ &childev);
2358	}	3019	}
2359	#endif	3020	#endif
…		…
2361	if (ev_is_active (&pipe_w))	3022	if (ev_is_active (&pipe_w))
2362	{	3023	{
2363	/*ev_ref (EV_A);*/	3024	/*ev_ref (EV_A);*/
2364	/*ev_io_stop (EV_A_ &pipe_w);*/	3025	/*ev_io_stop (EV_A_ &pipe_w);*/
2365		3026
2366	#if EV_USE_EVENTFD
2367	if (evfd >= 0)
2368	close (evfd);
2369	#endif
2370
2371	if (evpipe [0] >= 0)
2372	{
2373	EV_WIN32_CLOSE_FD (evpipe [0]);	3027	if (evpipe [0] >= 0) EV_WIN32_CLOSE_FD (evpipe [0]);
2374	EV_WIN32_CLOSE_FD (evpipe [1]);	3028	if (evpipe [1] >= 0) EV_WIN32_CLOSE_FD (evpipe [1]);
2375	}
2376	}	3029	}
2377		3030
2378	#if EV_USE_SIGNALFD	3031	#if EV_USE_SIGNALFD
2379	if (ev_is_active (&sigfd_w))	3032	if (ev_is_active (&sigfd_w))
2380	close (sigfd);	3033	close (sigfd);
…		…
2387		3040
2388	if (backend_fd >= 0)	3041	if (backend_fd >= 0)
2389	close (backend_fd);	3042	close (backend_fd);
2390		3043
2391	#if EV_USE_IOCP	3044	#if EV_USE_IOCP
2392	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);	3045	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);
2393	#endif	3046	#endif
2394	#if EV_USE_PORT	3047	#if EV_USE_PORT
2395	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);	3048	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);
2396	#endif	3049	#endif
2397	#if EV_USE_KQUEUE	3050	#if EV_USE_KQUEUE
2398	if (backend == EVBACKEND_KQUEUE) kqueue_destroy (EV_A);	3051	if (backend == EVBACKEND_KQUEUE ) kqueue_destroy (EV_A);
		3052	#endif
		3053	#if EV_USE_LINUXAIO
		3054	if (backend == EVBACKEND_LINUXAIO) linuxaio_destroy (EV_A);
2399	#endif	3055	#endif
2400	#if EV_USE_EPOLL	3056	#if EV_USE_EPOLL
2401	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);	3057	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);
2402	#endif	3058	#endif
2403	#if EV_USE_POLL	3059	#if EV_USE_POLL
2404	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);	3060	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);
2405	#endif	3061	#endif
2406	#if EV_USE_SELECT	3062	#if EV_USE_SELECT
2407	if (backend == EVBACKEND_SELECT) select_destroy (EV_A);	3063	if (backend == EVBACKEND_SELECT ) select_destroy (EV_A);
2408	#endif	3064	#endif
2409		3065
2410	for (i = NUMPRI; i--; )	3066	for (i = NUMPRI; i--; )
2411	{	3067	{
2412	array_free (pending, [i]);	3068	array_free (pending, [i]);
…		…
2454		3110
2455	inline_size void	3111	inline_size void
2456	loop_fork (EV_P)	3112	loop_fork (EV_P)
2457	{	3113	{
2458	#if EV_USE_PORT	3114	#if EV_USE_PORT
2459	if (backend == EVBACKEND_PORT ) port_fork (EV_A);	3115	if (backend == EVBACKEND_PORT ) port_fork (EV_A);
2460	#endif	3116	#endif
2461	#if EV_USE_KQUEUE	3117	#if EV_USE_KQUEUE
2462	if (backend == EVBACKEND_KQUEUE) kqueue_fork (EV_A);	3118	if (backend == EVBACKEND_KQUEUE ) kqueue_fork (EV_A);
		3119	#endif
		3120	#if EV_USE_LINUXAIO
		3121	if (backend == EVBACKEND_LINUXAIO) linuxaio_fork (EV_A);
2463	#endif	3122	#endif
2464	#if EV_USE_EPOLL	3123	#if EV_USE_EPOLL
2465	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);	3124	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);
2466	#endif	3125	#endif
2467	#if EV_USE_INOTIFY	3126	#if EV_USE_INOTIFY
2468	infy_fork (EV_A);	3127	infy_fork (EV_A);
2469	#endif	3128	#endif
2470		3129
		3130	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2471	if (ev_is_active (&pipe_w))	3131	if (ev_is_active (&pipe_w) && postfork != 2)
2472	{	3132	{
2473	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */	3133	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */
2474		3134
2475	ev_ref (EV_A);	3135	ev_ref (EV_A);
2476	ev_io_stop (EV_A_ &pipe_w);	3136	ev_io_stop (EV_A_ &pipe_w);
2477		3137
2478	#if EV_USE_EVENTFD
2479	if (evfd >= 0)
2480	close (evfd);
2481	#endif
2482
2483	if (evpipe [0] >= 0)	3138	if (evpipe [0] >= 0)
2484	{
2485	EV_WIN32_CLOSE_FD (evpipe [0]);	3139	EV_WIN32_CLOSE_FD (evpipe [0]);
2486	EV_WIN32_CLOSE_FD (evpipe [1]);
2487	}
2488		3140
2489	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2490	evpipe_init (EV_A);	3141	evpipe_init (EV_A);
2491	/* now iterate over everything, in case we missed something */	3142	/* iterate over everything, in case we missed something before */
2492	pipecb (EV_A_ &pipe_w, EV_READ);	3143	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);
2493	#endif
2494	}	3144	}
		3145	#endif
2495		3146
2496	postfork = 0;	3147	postfork = 0;
2497	}	3148	}
2498		3149
2499	#if EV_MULTIPLICITY	3150	#if EV_MULTIPLICITY
2500		3151
		3152	ecb_cold
2501	struct ev_loop * ecb_cold	3153	struct ev_loop *
2502	ev_loop_new (unsigned int flags) EV_THROW	3154	ev_loop_new (unsigned int flags) EV_NOEXCEPT
2503	{	3155	{
2504	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));	3156	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));
2505		3157
2506	memset (EV_A, 0, sizeof (struct ev_loop));	3158	memset (EV_A, 0, sizeof (struct ev_loop));
2507	loop_init (EV_A_ flags);	3159	loop_init (EV_A_ flags);
…		…
2514	}	3166	}
2515		3167
2516	#endif /* multiplicity */	3168	#endif /* multiplicity */
2517		3169
2518	#if EV_VERIFY	3170	#if EV_VERIFY
2519	static void noinline ecb_cold	3171	noinline ecb_cold
		3172	static void
2520	verify_watcher (EV_P_ W w)	3173	verify_watcher (EV_P_ W w)
2521	{	3174	{
2522	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));	3175	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));
2523		3176
2524	if (w->pending)	3177	if (w->pending)
2525	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));	3178	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));
2526	}	3179	}
2527		3180
2528	static void noinline ecb_cold	3181	noinline ecb_cold
		3182	static void
2529	verify_heap (EV_P_ ANHE *heap, int N)	3183	verify_heap (EV_P_ ANHE *heap, int N)
2530	{	3184	{
2531	int i;	3185	int i;
2532		3186
2533	for (i = HEAP0; i < N + HEAP0; ++i)	3187	for (i = HEAP0; i < N + HEAP0; ++i)
…		…
2538		3192
2539	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));	3193	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));
2540	}	3194	}
2541	}	3195	}
2542		3196
2543	static void noinline ecb_cold	3197	noinline ecb_cold
		3198	static void
2544	array_verify (EV_P_ W *ws, int cnt)	3199	array_verify (EV_P_ W *ws, int cnt)
2545	{	3200	{
2546	while (cnt--)	3201	while (cnt--)
2547	{	3202	{
2548	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));	3203	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));
…		…
2551	}	3206	}
2552	#endif	3207	#endif
2553		3208
2554	#if EV_FEATURE_API	3209	#if EV_FEATURE_API
2555	void ecb_cold	3210	void ecb_cold
2556	ev_verify (EV_P) EV_THROW	3211	ev_verify (EV_P) EV_NOEXCEPT
2557	{	3212	{
2558	#if EV_VERIFY	3213	#if EV_VERIFY
2559	int i, j;	3214	int i;
2560	WL w, w2;	3215	WL w, w2;
2561		3216
2562	assert (activecnt >= -1);	3217	assert (activecnt >= -1);
2563		3218
2564	assert (fdchangemax >= fdchangecnt);	3219	assert (fdchangemax >= fdchangecnt);
2565	for (i = 0; i < fdchangecnt; ++i)	3220	for (i = 0; i < fdchangecnt; ++i)
2566	assert (("libev: negative fd in fdchanges", fdchanges [i] >= 0));	3221	assert (("libev: negative fd in fdchanges", fdchanges [i] >= 0));
2567		3222
2568	assert (anfdmax >= 0);	3223	assert (anfdmax >= 0);
2569	for (i = j = 0; i < anfdmax; ++i)	3224	for (i = 0; i < anfdmax; ++i)
		3225	{
		3226	int j = 0;
		3227
2570	for (w = w2 = anfds [i].head; w; w = w->next)	3228	for (w = w2 = anfds [i].head; w; w = w->next)
2571	{	3229	{
2572	verify_watcher (EV_A_ (W)w);	3230	verify_watcher (EV_A_ (W)w);
2573		3231
2574	if (++j & 1)	3232	if (j++ & 1)
2575	w2 = w2->next;	3233	{
2576
2577	assert (("libev: io watcher list contains a loop", w != w2));	3234	assert (("libev: io watcher list contains a loop", w != w2));
		3235	w2 = w2->next;
		3236	}
		3237
2578	assert (("libev: inactive fd watcher on anfd list", ev_active (w) == 1));	3238	assert (("libev: inactive fd watcher on anfd list", ev_active (w) == 1));
2579	assert (("libev: fd mismatch between watcher and anfd", ((ev_io *)w)->fd == i));	3239	assert (("libev: fd mismatch between watcher and anfd", ((ev_io *)w)->fd == i));
2580	}	3240	}
		3241	}
2581		3242
2582	assert (timermax >= timercnt);	3243	assert (timermax >= timercnt);
2583	verify_heap (EV_A_ timers, timercnt);	3244	verify_heap (EV_A_ timers, timercnt);
2584		3245
2585	#if EV_PERIODIC_ENABLE	3246	#if EV_PERIODIC_ENABLE
…		…
2631	#endif	3292	#endif
2632	}	3293	}
2633	#endif	3294	#endif
2634		3295
2635	#if EV_MULTIPLICITY	3296	#if EV_MULTIPLICITY
		3297	ecb_cold
2636	struct ev_loop * ecb_cold	3298	struct ev_loop *
2637	#else	3299	#else
2638	int	3300	int
2639	#endif	3301	#endif
2640	ev_default_loop (unsigned int flags) EV_THROW	3302	ev_default_loop (unsigned int flags) EV_NOEXCEPT
2641	{	3303	{
2642	if (!ev_default_loop_ptr)	3304	if (!ev_default_loop_ptr)
2643	{	3305	{
2644	#if EV_MULTIPLICITY	3306	#if EV_MULTIPLICITY
2645	EV_P = ev_default_loop_ptr = &default_loop_struct;	3307	EV_P = ev_default_loop_ptr = &default_loop_struct;
…		…
2664		3326
2665	return ev_default_loop_ptr;	3327	return ev_default_loop_ptr;
2666	}	3328	}
2667		3329
2668	void	3330	void
2669	ev_loop_fork (EV_P) EV_THROW	3331	ev_loop_fork (EV_P) EV_NOEXCEPT
2670	{	3332	{
2671	postfork = 1; /* must be in line with ev_default_fork */	3333	postfork = 1;
2672	}	3334	}
2673		3335
2674	/*****************************************************************************/	3336	/*****************************************************************************/
2675		3337
2676	void	3338	void
…		…
2678	{	3340	{
2679	EV_CB_INVOKE ((W)w, revents);	3341	EV_CB_INVOKE ((W)w, revents);
2680	}	3342	}
2681		3343
2682	unsigned int	3344	unsigned int
2683	ev_pending_count (EV_P) EV_THROW	3345	ev_pending_count (EV_P) EV_NOEXCEPT
2684	{	3346	{
2685	int pri;	3347	int pri;
2686	unsigned int count = 0;	3348	unsigned int count = 0;
2687		3349
2688	for (pri = NUMPRI; pri--; )	3350	for (pri = NUMPRI; pri--; )
2689	count += pendingcnt [pri];	3351	count += pendingcnt [pri];
2690		3352
2691	return count;	3353	return count;
2692	}	3354	}
2693		3355
2694	void noinline	3356	noinline
		3357	void
2695	ev_invoke_pending (EV_P)	3358	ev_invoke_pending (EV_P)
2696	{	3359	{
2697	for (pendingpri = NUMPRI; pendingpri--; ) /* pendingpri is modified during the loop */	3360	pendingpri = NUMPRI;
		3361
		3362	do
		3363	{
		3364	--pendingpri;
		3365
		3366	/* pendingpri possibly gets modified in the inner loop */
2698	while (pendingcnt [pendingpri])	3367	while (pendingcnt [pendingpri])
2699	{	3368	{
2700	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];	3369	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];
2701		3370
2702	p->w->pending = 0;	3371	p->w->pending = 0;
2703	EV_CB_INVOKE (p->w, p->events);	3372	EV_CB_INVOKE (p->w, p->events);
2704	EV_FREQUENT_CHECK;	3373	EV_FREQUENT_CHECK;
2705	}	3374	}
		3375	}
		3376	while (pendingpri);
2706	}	3377	}
2707		3378
2708	#if EV_IDLE_ENABLE	3379	#if EV_IDLE_ENABLE
2709	/* make idle watchers pending. this handles the "call-idle */	3380	/* make idle watchers pending. this handles the "call-idle */
2710	/* only when higher priorities are idle" logic */	3381	/* only when higher priorities are idle" logic */
…		…
2768	}	3439	}
2769	}	3440	}
2770		3441
2771	#if EV_PERIODIC_ENABLE	3442	#if EV_PERIODIC_ENABLE
2772		3443
2773	static void noinline	3444	noinline
		3445	static void
2774	periodic_recalc (EV_P_ ev_periodic *w)	3446	periodic_recalc (EV_P_ ev_periodic *w)
2775	{	3447	{
2776	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;	3448	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;
2777	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);	3449	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);
2778		3450
…		…
2800	{	3472	{
2801	EV_FREQUENT_CHECK;	3473	EV_FREQUENT_CHECK;
2802		3474
2803	while (periodiccnt && ANHE_at (periodics [HEAP0]) < ev_rt_now)	3475	while (periodiccnt && ANHE_at (periodics [HEAP0]) < ev_rt_now)
2804	{	3476	{
2805	int feed_count = 0;
2806
2807	do	3477	do
2808	{	3478	{
2809	ev_periodic *w = (ev_periodic *)ANHE_w (periodics [HEAP0]);	3479	ev_periodic *w = (ev_periodic *)ANHE_w (periodics [HEAP0]);
2810		3480
2811	/*assert (("libev: inactive timer on periodic heap detected", ev_is_active (w)));*/	3481	/*assert (("libev: inactive timer on periodic heap detected", ev_is_active (w)));*/
…		…
2838	}	3508	}
2839	}	3509	}
2840		3510
2841	/* simply recalculate all periodics */	3511	/* simply recalculate all periodics */
2842	/* TODO: maybe ensure that at least one event happens when jumping forward? */	3512	/* TODO: maybe ensure that at least one event happens when jumping forward? */
2843	static void noinline ecb_cold	3513	noinline ecb_cold
		3514	static void
2844	periodics_reschedule (EV_P)	3515	periodics_reschedule (EV_P)
2845	{	3516	{
2846	int i;	3517	int i;
2847		3518
2848	/* adjust periodics after time jump */	3519	/* adjust periodics after time jump */
…		…
2861	reheap (periodics, periodiccnt);	3532	reheap (periodics, periodiccnt);
2862	}	3533	}
2863	#endif	3534	#endif
2864		3535
2865	/* adjust all timers by a given offset */	3536	/* adjust all timers by a given offset */
2866	static void noinline ecb_cold	3537	noinline ecb_cold
		3538	static void
2867	timers_reschedule (EV_P_ ev_tstamp adjust)	3539	timers_reschedule (EV_P_ ev_tstamp adjust)
2868	{	3540	{
2869	int i;	3541	int i;
2870		3542
2871	for (i = 0; i < timercnt; ++i)	3543	for (i = 0; i < timercnt; ++i)
…		…
3070	backend_poll (EV_A_ waittime);	3742	backend_poll (EV_A_ waittime);
3071	assert ((loop_done = EVBREAK_CANCEL, 1)); /* assert for side effect */	3743	assert ((loop_done = EVBREAK_CANCEL, 1)); /* assert for side effect */
3072		3744
3073	pipe_write_wanted = 0; /* just an optimisation, no fence needed */	3745	pipe_write_wanted = 0; /* just an optimisation, no fence needed */
3074		3746
		3747	ECB_MEMORY_FENCE_ACQUIRE;
3075	if (pipe_write_skipped)	3748	if (pipe_write_skipped)
3076	{	3749	{
3077	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));	3750	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));
3078	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);	3751	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);
3079	}	3752	}
…		…
3117		3790
3118	return activecnt;	3791	return activecnt;
3119	}	3792	}
3120		3793
3121	void	3794	void
3122	ev_break (EV_P_ int how) EV_THROW	3795	ev_break (EV_P_ int how) EV_NOEXCEPT
3123	{	3796	{
3124	loop_done = how;	3797	loop_done = how;
3125	}	3798	}
3126		3799
3127	void	3800	void
3128	ev_ref (EV_P) EV_THROW	3801	ev_ref (EV_P) EV_NOEXCEPT
3129	{	3802	{
3130	++activecnt;	3803	++activecnt;
3131	}	3804	}
3132		3805
3133	void	3806	void
3134	ev_unref (EV_P) EV_THROW	3807	ev_unref (EV_P) EV_NOEXCEPT
3135	{	3808	{
3136	--activecnt;	3809	--activecnt;
3137	}	3810	}
3138		3811
3139	void	3812	void
3140	ev_now_update (EV_P) EV_THROW	3813	ev_now_update (EV_P) EV_NOEXCEPT
3141	{	3814	{
3142	time_update (EV_A_ 1e100);	3815	time_update (EV_A_ 1e100);
3143	}	3816	}
3144		3817
3145	void	3818	void
3146	ev_suspend (EV_P) EV_THROW	3819	ev_suspend (EV_P) EV_NOEXCEPT
3147	{	3820	{
3148	ev_now_update (EV_A);	3821	ev_now_update (EV_A);
3149	}	3822	}
3150		3823
3151	void	3824	void
3152	ev_resume (EV_P) EV_THROW	3825	ev_resume (EV_P) EV_NOEXCEPT
3153	{	3826	{
3154	ev_tstamp mn_prev = mn_now;	3827	ev_tstamp mn_prev = mn_now;
3155		3828
3156	ev_now_update (EV_A);	3829	ev_now_update (EV_A);
3157	timers_reschedule (EV_A_ mn_now - mn_prev);	3830	timers_reschedule (EV_A_ mn_now - mn_prev);
…		…
3196	w->pending = 0;	3869	w->pending = 0;
3197	}	3870	}
3198	}	3871	}
3199		3872
3200	int	3873	int
3201	ev_clear_pending (EV_P_ void *w) EV_THROW	3874	ev_clear_pending (EV_P_ void *w) EV_NOEXCEPT
3202	{	3875	{
3203	W w_ = (W)w;	3876	W w_ = (W)w;
3204	int pending = w_->pending;	3877	int pending = w_->pending;
3205		3878
3206	if (expect_true (pending))	3879	if (expect_true (pending))
…		…
3238	w->active = 0;	3911	w->active = 0;
3239	}	3912	}
3240		3913
3241	/*****************************************************************************/	3914	/*****************************************************************************/
3242		3915
3243	void noinline	3916	noinline
		3917	void
3244	ev_io_start (EV_P_ ev_io *w) EV_THROW	3918	ev_io_start (EV_P_ ev_io *w) EV_NOEXCEPT
3245	{	3919	{
3246	int fd = w->fd;	3920	int fd = w->fd;
3247		3921
3248	if (expect_false (ev_is_active (w)))	3922	if (expect_false (ev_is_active (w)))
3249	return;	3923	return;
3250		3924
3251	assert (("libev: ev_io_start called with negative fd", fd >= 0));	3925	assert (("libev: ev_io_start called with negative fd", fd >= 0));
3252	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));	3926	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));
3253		3927
		3928	#if EV_VERIFY >= 2
		3929	assert (("libev: ev_io_start called on watcher with invalid fd", fd_valid (fd)));
		3930	#endif
3254	EV_FREQUENT_CHECK;	3931	EV_FREQUENT_CHECK;
3255		3932
3256	ev_start (EV_A_ (W)w, 1);	3933	ev_start (EV_A_ (W)w, 1);
3257	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_init_zero);	3934	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_needsize_zerofill);
3258	wlist_add (&anfds[fd].head, (WL)w);	3935	wlist_add (&anfds[fd].head, (WL)w);
3259		3936
3260	/* common bug, apparently */	3937	/* common bug, apparently */
3261	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));	3938	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));
3262		3939
…		…
3264	w->events &= ~EV__IOFDSET;	3941	w->events &= ~EV__IOFDSET;
3265		3942
3266	EV_FREQUENT_CHECK;	3943	EV_FREQUENT_CHECK;
3267	}	3944	}
3268		3945
3269	void noinline	3946	noinline
		3947	void
3270	ev_io_stop (EV_P_ ev_io *w) EV_THROW	3948	ev_io_stop (EV_P_ ev_io *w) EV_NOEXCEPT
3271	{	3949	{
3272	clear_pending (EV_A_ (W)w);	3950	clear_pending (EV_A_ (W)w);
3273	if (expect_false (!ev_is_active (w)))	3951	if (expect_false (!ev_is_active (w)))
3274	return;	3952	return;
3275		3953
3276	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));	3954	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));
3277		3955
		3956	#if EV_VERIFY >= 2
		3957	assert (("libev: ev_io_stop called on watcher with invalid fd", fd_valid (w->fd)));
		3958	#endif
3278	EV_FREQUENT_CHECK;	3959	EV_FREQUENT_CHECK;
3279		3960
3280	wlist_del (&anfds[w->fd].head, (WL)w);	3961	wlist_del (&anfds[w->fd].head, (WL)w);
3281	ev_stop (EV_A_ (W)w);	3962	ev_stop (EV_A_ (W)w);
3282		3963
3283	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);	3964	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);
3284		3965
3285	EV_FREQUENT_CHECK;	3966	EV_FREQUENT_CHECK;
3286	}	3967	}
3287		3968
3288	void noinline	3969	noinline
		3970	void
3289	ev_timer_start (EV_P_ ev_timer *w) EV_THROW	3971	ev_timer_start (EV_P_ ev_timer *w) EV_NOEXCEPT
3290	{	3972	{
3291	if (expect_false (ev_is_active (w)))	3973	if (expect_false (ev_is_active (w)))
3292	return;	3974	return;
3293		3975
3294	ev_at (w) += mn_now;	3976	ev_at (w) += mn_now;
…		…
3297		3979
3298	EV_FREQUENT_CHECK;	3980	EV_FREQUENT_CHECK;
3299		3981
3300	++timercnt;	3982	++timercnt;
3301	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);	3983	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);
3302	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, EMPTY2);	3984	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, array_needsize_noinit);
3303	ANHE_w (timers [ev_active (w)]) = (WT)w;	3985	ANHE_w (timers [ev_active (w)]) = (WT)w;
3304	ANHE_at_cache (timers [ev_active (w)]);	3986	ANHE_at_cache (timers [ev_active (w)]);
3305	upheap (timers, ev_active (w));	3987	upheap (timers, ev_active (w));
3306		3988
3307	EV_FREQUENT_CHECK;	3989	EV_FREQUENT_CHECK;
3308		3990
3309	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/	3991	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/
3310	}	3992	}
3311		3993
3312	void noinline	3994	noinline
		3995	void
3313	ev_timer_stop (EV_P_ ev_timer *w) EV_THROW	3996	ev_timer_stop (EV_P_ ev_timer *w) EV_NOEXCEPT
3314	{	3997	{
3315	clear_pending (EV_A_ (W)w);	3998	clear_pending (EV_A_ (W)w);
3316	if (expect_false (!ev_is_active (w)))	3999	if (expect_false (!ev_is_active (w)))
3317	return;	4000	return;
3318		4001
…		…
3337	ev_stop (EV_A_ (W)w);	4020	ev_stop (EV_A_ (W)w);
3338		4021
3339	EV_FREQUENT_CHECK;	4022	EV_FREQUENT_CHECK;
3340	}	4023	}
3341		4024
3342	void noinline	4025	noinline
		4026	void
3343	ev_timer_again (EV_P_ ev_timer *w) EV_THROW	4027	ev_timer_again (EV_P_ ev_timer *w) EV_NOEXCEPT
3344	{	4028	{
3345	EV_FREQUENT_CHECK;	4029	EV_FREQUENT_CHECK;
3346		4030
3347	clear_pending (EV_A_ (W)w);	4031	clear_pending (EV_A_ (W)w);
3348		4032
…		…
3365		4049
3366	EV_FREQUENT_CHECK;	4050	EV_FREQUENT_CHECK;
3367	}	4051	}
3368		4052
3369	ev_tstamp	4053	ev_tstamp
3370	ev_timer_remaining (EV_P_ ev_timer *w) EV_THROW	4054	ev_timer_remaining (EV_P_ ev_timer *w) EV_NOEXCEPT
3371	{	4055	{
3372	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);	4056	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);
3373	}	4057	}
3374		4058
3375	#if EV_PERIODIC_ENABLE	4059	#if EV_PERIODIC_ENABLE
3376	void noinline	4060	noinline
		4061	void
3377	ev_periodic_start (EV_P_ ev_periodic *w) EV_THROW	4062	ev_periodic_start (EV_P_ ev_periodic *w) EV_NOEXCEPT
3378	{	4063	{
3379	if (expect_false (ev_is_active (w)))	4064	if (expect_false (ev_is_active (w)))
3380	return;	4065	return;
3381		4066
3382	if (w->reschedule_cb)	4067	if (w->reschedule_cb)
…		…
3391		4076
3392	EV_FREQUENT_CHECK;	4077	EV_FREQUENT_CHECK;
3393		4078
3394	++periodiccnt;	4079	++periodiccnt;
3395	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);	4080	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);
3396	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, EMPTY2);	4081	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, array_needsize_noinit);
3397	ANHE_w (periodics [ev_active (w)]) = (WT)w;	4082	ANHE_w (periodics [ev_active (w)]) = (WT)w;
3398	ANHE_at_cache (periodics [ev_active (w)]);	4083	ANHE_at_cache (periodics [ev_active (w)]);
3399	upheap (periodics, ev_active (w));	4084	upheap (periodics, ev_active (w));
3400		4085
3401	EV_FREQUENT_CHECK;	4086	EV_FREQUENT_CHECK;
3402		4087
3403	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/	4088	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/
3404	}	4089	}
3405		4090
3406	void noinline	4091	noinline
		4092	void
3407	ev_periodic_stop (EV_P_ ev_periodic *w) EV_THROW	4093	ev_periodic_stop (EV_P_ ev_periodic *w) EV_NOEXCEPT
3408	{	4094	{
3409	clear_pending (EV_A_ (W)w);	4095	clear_pending (EV_A_ (W)w);
3410	if (expect_false (!ev_is_active (w)))	4096	if (expect_false (!ev_is_active (w)))
3411	return;	4097	return;
3412		4098
…		…
3429	ev_stop (EV_A_ (W)w);	4115	ev_stop (EV_A_ (W)w);
3430		4116
3431	EV_FREQUENT_CHECK;	4117	EV_FREQUENT_CHECK;
3432	}	4118	}
3433		4119
3434	void noinline	4120	noinline
		4121	void
3435	ev_periodic_again (EV_P_ ev_periodic *w) EV_THROW	4122	ev_periodic_again (EV_P_ ev_periodic *w) EV_NOEXCEPT
3436	{	4123	{
3437	/* TODO: use adjustheap and recalculation */	4124	/* TODO: use adjustheap and recalculation */
3438	ev_periodic_stop (EV_A_ w);	4125	ev_periodic_stop (EV_A_ w);
3439	ev_periodic_start (EV_A_ w);	4126	ev_periodic_start (EV_A_ w);
3440	}	4127	}
…		…
3444	# define SA_RESTART 0	4131	# define SA_RESTART 0
3445	#endif	4132	#endif
3446		4133
3447	#if EV_SIGNAL_ENABLE	4134	#if EV_SIGNAL_ENABLE
3448		4135
3449	void noinline	4136	noinline
		4137	void
3450	ev_signal_start (EV_P_ ev_signal *w) EV_THROW	4138	ev_signal_start (EV_P_ ev_signal *w) EV_NOEXCEPT
3451	{	4139	{
3452	if (expect_false (ev_is_active (w)))	4140	if (expect_false (ev_is_active (w)))
3453	return;	4141	return;
3454		4142
3455	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));	4143	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));
…		…
3457	#if EV_MULTIPLICITY	4145	#if EV_MULTIPLICITY
3458	assert (("libev: a signal must not be attached to two different loops",	4146	assert (("libev: a signal must not be attached to two different loops",
3459	!signals [w->signum - 1].loop || signals [w->signum - 1].loop == loop));	4147	!signals [w->signum - 1].loop || signals [w->signum - 1].loop == loop));
3460		4148
3461	signals [w->signum - 1].loop = EV_A;	4149	signals [w->signum - 1].loop = EV_A;
		4150	ECB_MEMORY_FENCE_RELEASE;
3462	#endif	4151	#endif
3463		4152
3464	EV_FREQUENT_CHECK;	4153	EV_FREQUENT_CHECK;
3465		4154
3466	#if EV_USE_SIGNALFD	4155	#if EV_USE_SIGNALFD
…		…
3525	}	4214	}
3526		4215
3527	EV_FREQUENT_CHECK;	4216	EV_FREQUENT_CHECK;
3528	}	4217	}
3529		4218
3530	void noinline	4219	noinline
		4220	void
3531	ev_signal_stop (EV_P_ ev_signal *w) EV_THROW	4221	ev_signal_stop (EV_P_ ev_signal *w) EV_NOEXCEPT
3532	{	4222	{
3533	clear_pending (EV_A_ (W)w);	4223	clear_pending (EV_A_ (W)w);
3534	if (expect_false (!ev_is_active (w)))	4224	if (expect_false (!ev_is_active (w)))
3535	return;	4225	return;
3536		4226
…		…
3567	#endif	4257	#endif
3568		4258
3569	#if EV_CHILD_ENABLE	4259	#if EV_CHILD_ENABLE
3570		4260
3571	void	4261	void
3572	ev_child_start (EV_P_ ev_child *w) EV_THROW	4262	ev_child_start (EV_P_ ev_child *w) EV_NOEXCEPT
3573	{	4263	{
3574	#if EV_MULTIPLICITY	4264	#if EV_MULTIPLICITY
3575	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));	4265	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));
3576	#endif	4266	#endif
3577	if (expect_false (ev_is_active (w)))	4267	if (expect_false (ev_is_active (w)))
…		…
3584		4274
3585	EV_FREQUENT_CHECK;	4275	EV_FREQUENT_CHECK;
3586	}	4276	}
3587		4277
3588	void	4278	void
3589	ev_child_stop (EV_P_ ev_child *w) EV_THROW	4279	ev_child_stop (EV_P_ ev_child *w) EV_NOEXCEPT
3590	{	4280	{
3591	clear_pending (EV_A_ (W)w);	4281	clear_pending (EV_A_ (W)w);
3592	if (expect_false (!ev_is_active (w)))	4282	if (expect_false (!ev_is_active (w)))
3593	return;	4283	return;
3594		4284
…		…
3611		4301
3612	#define DEF_STAT_INTERVAL 5.0074891	4302	#define DEF_STAT_INTERVAL 5.0074891
3613	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */	4303	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */
3614	#define MIN_STAT_INTERVAL 0.1074891	4304	#define MIN_STAT_INTERVAL 0.1074891
3615		4305
3616	static void noinline stat_timer_cb (EV_P_ ev_timer *w_, int revents);	4306	noinline static void stat_timer_cb (EV_P_ ev_timer *w_, int revents);
3617		4307
3618	#if EV_USE_INOTIFY	4308	#if EV_USE_INOTIFY
3619		4309
3620	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */	4310	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */
3621	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)	4311	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)
3622		4312
3623	static void noinline	4313	noinline
		4314	static void
3624	infy_add (EV_P_ ev_stat *w)	4315	infy_add (EV_P_ ev_stat *w)
3625	{	4316	{
3626	w->wd = inotify_add_watch (fs_fd, w->path, IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY | IN_DONT_FOLLOW | IN_MASK_ADD);	4317	w->wd = inotify_add_watch (fs_fd, w->path,
		4318	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY
		4319	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO
		4320	| IN_DONT_FOLLOW | IN_MASK_ADD);
3627		4321
3628	if (w->wd >= 0)	4322	if (w->wd >= 0)
3629	{	4323	{
3630	struct statfs sfs;	4324	struct statfs sfs;
3631		4325
…		…
3635		4329
3636	if (!fs_2625)	4330	if (!fs_2625)
3637	w->timer.repeat = w->interval ? w->interval : DEF_STAT_INTERVAL;	4331	w->timer.repeat = w->interval ? w->interval : DEF_STAT_INTERVAL;
3638	else if (!statfs (w->path, &sfs)	4332	else if (!statfs (w->path, &sfs)
3639	&& (sfs.f_type == 0x1373 /* devfs */	4333	&& (sfs.f_type == 0x1373 /* devfs */
		4334	|| sfs.f_type == 0x4006 /* fat */
		4335	|| sfs.f_type == 0x4d44 /* msdos */
3640	|| sfs.f_type == 0xEF53 /* ext2/3 */	4336	|| sfs.f_type == 0xEF53 /* ext2/3 */
		4337	|| sfs.f_type == 0x72b6 /* jffs2 */
		4338	|| sfs.f_type == 0x858458f6 /* ramfs */
		4339	|| sfs.f_type == 0x5346544e /* ntfs */
3641	|| sfs.f_type == 0x3153464a /* jfs */	4340	|| sfs.f_type == 0x3153464a /* jfs */
		4341	|| sfs.f_type == 0x9123683e /* btrfs */
3642	|| sfs.f_type == 0x52654973 /* reiser3 */	4342	|| sfs.f_type == 0x52654973 /* reiser3 */
3643	|| sfs.f_type == 0x01021994 /* tempfs */	4343	|| sfs.f_type == 0x01021994 /* tmpfs */
3644	|| sfs.f_type == 0x58465342 /* xfs */))	4344	|| sfs.f_type == 0x58465342 /* xfs */))
3645	w->timer.repeat = 0.; /* filesystem is local, kernel new enough */	4345	w->timer.repeat = 0.; /* filesystem is local, kernel new enough */
3646	else	4346	else
3647	w->timer.repeat = w->interval ? w->interval : NFS_STAT_INTERVAL; /* remote, use reduced frequency */	4347	w->timer.repeat = w->interval ? w->interval : NFS_STAT_INTERVAL; /* remote, use reduced frequency */
3648	}	4348	}
…		…
3683	if (ev_is_active (&w->timer)) ev_ref (EV_A);	4383	if (ev_is_active (&w->timer)) ev_ref (EV_A);
3684	ev_timer_again (EV_A_ &w->timer);	4384	ev_timer_again (EV_A_ &w->timer);
3685	if (ev_is_active (&w->timer)) ev_unref (EV_A);	4385	if (ev_is_active (&w->timer)) ev_unref (EV_A);
3686	}	4386	}
3687		4387
3688	static void noinline	4388	noinline
		4389	static void
3689	infy_del (EV_P_ ev_stat *w)	4390	infy_del (EV_P_ ev_stat *w)
3690	{	4391	{
3691	int slot;	4392	int slot;
3692	int wd = w->wd;	4393	int wd = w->wd;
3693		4394
…		…
3700		4401
3701	/* remove this watcher, if others are watching it, they will rearm */	4402	/* remove this watcher, if others are watching it, they will rearm */
3702	inotify_rm_watch (fs_fd, wd);	4403	inotify_rm_watch (fs_fd, wd);
3703	}	4404	}
3704		4405
3705	static void noinline	4406	noinline
		4407	static void
3706	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)	4408	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)
3707	{	4409	{
3708	if (slot < 0)	4410	if (slot < 0)
3709	/* overflow, need to check for all hash slots */	4411	/* overflow, need to check for all hash slots */
3710	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)	4412	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)
…		…
3746	infy_wd (EV_A_ ev->wd, ev->wd, ev);	4448	infy_wd (EV_A_ ev->wd, ev->wd, ev);
3747	ofs += sizeof (struct inotify_event) + ev->len;	4449	ofs += sizeof (struct inotify_event) + ev->len;
3748	}	4450	}
3749	}	4451	}
3750		4452
3751	inline_size void ecb_cold	4453	inline_size ecb_cold
		4454	void
3752	ev_check_2625 (EV_P)	4455	ev_check_2625 (EV_P)
3753	{	4456	{
3754	/* kernels < 2.6.25 are borked	4457	/* kernels < 2.6.25 are borked
3755	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html	4458	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html
3756	*/	4459	*/
…		…
3846	#else	4549	#else
3847	# define EV_LSTAT(p,b) lstat (p, b)	4550	# define EV_LSTAT(p,b) lstat (p, b)
3848	#endif	4551	#endif
3849		4552
3850	void	4553	void
3851	ev_stat_stat (EV_P_ ev_stat *w) EV_THROW	4554	ev_stat_stat (EV_P_ ev_stat *w) EV_NOEXCEPT
3852	{	4555	{
3853	if (lstat (w->path, &w->attr) < 0)	4556	if (lstat (w->path, &w->attr) < 0)
3854	w->attr.st_nlink = 0;	4557	w->attr.st_nlink = 0;
3855	else if (!w->attr.st_nlink)	4558	else if (!w->attr.st_nlink)
3856	w->attr.st_nlink = 1;	4559	w->attr.st_nlink = 1;
3857	}	4560	}
3858		4561
3859	static void noinline	4562	noinline
		4563	static void
3860	stat_timer_cb (EV_P_ ev_timer *w_, int revents)	4564	stat_timer_cb (EV_P_ ev_timer *w_, int revents)
3861	{	4565	{
3862	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));	4566	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));
3863		4567
3864	ev_statdata prev = w->attr;	4568	ev_statdata prev = w->attr;
…		…
3895	ev_feed_event (EV_A_ w, EV_STAT);	4599	ev_feed_event (EV_A_ w, EV_STAT);
3896	}	4600	}
3897	}	4601	}
3898		4602
3899	void	4603	void
3900	ev_stat_start (EV_P_ ev_stat *w) EV_THROW	4604	ev_stat_start (EV_P_ ev_stat *w) EV_NOEXCEPT
3901	{	4605	{
3902	if (expect_false (ev_is_active (w)))	4606	if (expect_false (ev_is_active (w)))
3903	return;	4607	return;
3904		4608
3905	ev_stat_stat (EV_A_ w);	4609	ev_stat_stat (EV_A_ w);
…		…
3926		4630
3927	EV_FREQUENT_CHECK;	4631	EV_FREQUENT_CHECK;
3928	}	4632	}
3929		4633
3930	void	4634	void
3931	ev_stat_stop (EV_P_ ev_stat *w) EV_THROW	4635	ev_stat_stop (EV_P_ ev_stat *w) EV_NOEXCEPT
3932	{	4636	{
3933	clear_pending (EV_A_ (W)w);	4637	clear_pending (EV_A_ (W)w);
3934	if (expect_false (!ev_is_active (w)))	4638	if (expect_false (!ev_is_active (w)))
3935	return;	4639	return;
3936		4640
…		…
3952	}	4656	}
3953	#endif	4657	#endif
3954		4658
3955	#if EV_IDLE_ENABLE	4659	#if EV_IDLE_ENABLE
3956	void	4660	void
3957	ev_idle_start (EV_P_ ev_idle *w) EV_THROW	4661	ev_idle_start (EV_P_ ev_idle *w) EV_NOEXCEPT
3958	{	4662	{
3959	if (expect_false (ev_is_active (w)))	4663	if (expect_false (ev_is_active (w)))
3960	return;	4664	return;
3961		4665
3962	pri_adjust (EV_A_ (W)w);	4666	pri_adjust (EV_A_ (W)w);
…		…
3967	int active = ++idlecnt [ABSPRI (w)];	4671	int active = ++idlecnt [ABSPRI (w)];
3968		4672
3969	++idleall;	4673	++idleall;
3970	ev_start (EV_A_ (W)w, active);	4674	ev_start (EV_A_ (W)w, active);
3971		4675
3972	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, EMPTY2);	4676	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, array_needsize_noinit);
3973	idles [ABSPRI (w)][active - 1] = w;	4677	idles [ABSPRI (w)][active - 1] = w;
3974	}	4678	}
3975		4679
3976	EV_FREQUENT_CHECK;	4680	EV_FREQUENT_CHECK;
3977	}	4681	}
3978		4682
3979	void	4683	void
3980	ev_idle_stop (EV_P_ ev_idle *w) EV_THROW	4684	ev_idle_stop (EV_P_ ev_idle *w) EV_NOEXCEPT
3981	{	4685	{
3982	clear_pending (EV_A_ (W)w);	4686	clear_pending (EV_A_ (W)w);
3983	if (expect_false (!ev_is_active (w)))	4687	if (expect_false (!ev_is_active (w)))
3984	return;	4688	return;
3985		4689
…		…
3999	}	4703	}
4000	#endif	4704	#endif
4001		4705
4002	#if EV_PREPARE_ENABLE	4706	#if EV_PREPARE_ENABLE
4003	void	4707	void
4004	ev_prepare_start (EV_P_ ev_prepare *w) EV_THROW	4708	ev_prepare_start (EV_P_ ev_prepare *w) EV_NOEXCEPT
4005	{	4709	{
4006	if (expect_false (ev_is_active (w)))	4710	if (expect_false (ev_is_active (w)))
4007	return;	4711	return;
4008		4712
4009	EV_FREQUENT_CHECK;	4713	EV_FREQUENT_CHECK;
4010		4714
4011	ev_start (EV_A_ (W)w, ++preparecnt);	4715	ev_start (EV_A_ (W)w, ++preparecnt);
4012	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, EMPTY2);	4716	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, array_needsize_noinit);
4013	prepares [preparecnt - 1] = w;	4717	prepares [preparecnt - 1] = w;
4014		4718
4015	EV_FREQUENT_CHECK;	4719	EV_FREQUENT_CHECK;
4016	}	4720	}
4017		4721
4018	void	4722	void
4019	ev_prepare_stop (EV_P_ ev_prepare *w) EV_THROW	4723	ev_prepare_stop (EV_P_ ev_prepare *w) EV_NOEXCEPT
4020	{	4724	{
4021	clear_pending (EV_A_ (W)w);	4725	clear_pending (EV_A_ (W)w);
4022	if (expect_false (!ev_is_active (w)))	4726	if (expect_false (!ev_is_active (w)))
4023	return;	4727	return;
4024		4728
…		…
4037	}	4741	}
4038	#endif	4742	#endif
4039		4743
4040	#if EV_CHECK_ENABLE	4744	#if EV_CHECK_ENABLE
4041	void	4745	void
4042	ev_check_start (EV_P_ ev_check *w) EV_THROW	4746	ev_check_start (EV_P_ ev_check *w) EV_NOEXCEPT
4043	{	4747	{
4044	if (expect_false (ev_is_active (w)))	4748	if (expect_false (ev_is_active (w)))
4045	return;	4749	return;
4046		4750
4047	EV_FREQUENT_CHECK;	4751	EV_FREQUENT_CHECK;
4048		4752
4049	ev_start (EV_A_ (W)w, ++checkcnt);	4753	ev_start (EV_A_ (W)w, ++checkcnt);
4050	array_needsize (ev_check *, checks, checkmax, checkcnt, EMPTY2);	4754	array_needsize (ev_check *, checks, checkmax, checkcnt, array_needsize_noinit);
4051	checks [checkcnt - 1] = w;	4755	checks [checkcnt - 1] = w;
4052		4756
4053	EV_FREQUENT_CHECK;	4757	EV_FREQUENT_CHECK;
4054	}	4758	}
4055		4759
4056	void	4760	void
4057	ev_check_stop (EV_P_ ev_check *w) EV_THROW	4761	ev_check_stop (EV_P_ ev_check *w) EV_NOEXCEPT
4058	{	4762	{
4059	clear_pending (EV_A_ (W)w);	4763	clear_pending (EV_A_ (W)w);
4060	if (expect_false (!ev_is_active (w)))	4764	if (expect_false (!ev_is_active (w)))
4061	return;	4765	return;
4062		4766
…		…
4074	EV_FREQUENT_CHECK;	4778	EV_FREQUENT_CHECK;
4075	}	4779	}
4076	#endif	4780	#endif
4077		4781
4078	#if EV_EMBED_ENABLE	4782	#if EV_EMBED_ENABLE
4079	void noinline	4783	noinline
		4784	void
4080	ev_embed_sweep (EV_P_ ev_embed *w) EV_THROW	4785	ev_embed_sweep (EV_P_ ev_embed *w) EV_NOEXCEPT
4081	{	4786	{
4082	ev_run (w->other, EVRUN_NOWAIT);	4787	ev_run (w->other, EVRUN_NOWAIT);
4083	}	4788	}
4084		4789
4085	static void	4790	static void
…		…
4133	ev_idle_stop (EV_A_ idle);	4838	ev_idle_stop (EV_A_ idle);
4134	}	4839	}
4135	#endif	4840	#endif
4136		4841
4137	void	4842	void
4138	ev_embed_start (EV_P_ ev_embed *w) EV_THROW	4843	ev_embed_start (EV_P_ ev_embed *w) EV_NOEXCEPT
4139	{	4844	{
4140	if (expect_false (ev_is_active (w)))	4845	if (expect_false (ev_is_active (w)))
4141	return;	4846	return;
4142		4847
4143	{	4848	{
…		…
4164		4869
4165	EV_FREQUENT_CHECK;	4870	EV_FREQUENT_CHECK;
4166	}	4871	}
4167		4872
4168	void	4873	void
4169	ev_embed_stop (EV_P_ ev_embed *w) EV_THROW	4874	ev_embed_stop (EV_P_ ev_embed *w) EV_NOEXCEPT
4170	{	4875	{
4171	clear_pending (EV_A_ (W)w);	4876	clear_pending (EV_A_ (W)w);
4172	if (expect_false (!ev_is_active (w)))	4877	if (expect_false (!ev_is_active (w)))
4173	return;	4878	return;
4174		4879
…		…
4184	}	4889	}
4185	#endif	4890	#endif
4186		4891
4187	#if EV_FORK_ENABLE	4892	#if EV_FORK_ENABLE
4188	void	4893	void
4189	ev_fork_start (EV_P_ ev_fork *w) EV_THROW	4894	ev_fork_start (EV_P_ ev_fork *w) EV_NOEXCEPT
4190	{	4895	{
4191	if (expect_false (ev_is_active (w)))	4896	if (expect_false (ev_is_active (w)))
4192	return;	4897	return;
4193		4898
4194	EV_FREQUENT_CHECK;	4899	EV_FREQUENT_CHECK;
4195		4900
4196	ev_start (EV_A_ (W)w, ++forkcnt);	4901	ev_start (EV_A_ (W)w, ++forkcnt);
4197	array_needsize (ev_fork *, forks, forkmax, forkcnt, EMPTY2);	4902	array_needsize (ev_fork *, forks, forkmax, forkcnt, array_needsize_noinit);
4198	forks [forkcnt - 1] = w;	4903	forks [forkcnt - 1] = w;
4199		4904
4200	EV_FREQUENT_CHECK;	4905	EV_FREQUENT_CHECK;
4201	}	4906	}
4202		4907
4203	void	4908	void
4204	ev_fork_stop (EV_P_ ev_fork *w) EV_THROW	4909	ev_fork_stop (EV_P_ ev_fork *w) EV_NOEXCEPT
4205	{	4910	{
4206	clear_pending (EV_A_ (W)w);	4911	clear_pending (EV_A_ (W)w);
4207	if (expect_false (!ev_is_active (w)))	4912	if (expect_false (!ev_is_active (w)))
4208	return;	4913	return;
4209		4914
…		…
4222	}	4927	}
4223	#endif	4928	#endif
4224		4929
4225	#if EV_CLEANUP_ENABLE	4930	#if EV_CLEANUP_ENABLE
4226	void	4931	void
4227	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_THROW	4932	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4228	{	4933	{
4229	if (expect_false (ev_is_active (w)))	4934	if (expect_false (ev_is_active (w)))
4230	return;	4935	return;
4231		4936
4232	EV_FREQUENT_CHECK;	4937	EV_FREQUENT_CHECK;
4233		4938
4234	ev_start (EV_A_ (W)w, ++cleanupcnt);	4939	ev_start (EV_A_ (W)w, ++cleanupcnt);
4235	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, EMPTY2);	4940	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, array_needsize_noinit);
4236	cleanups [cleanupcnt - 1] = w;	4941	cleanups [cleanupcnt - 1] = w;
4237		4942
4238	/* cleanup watchers should never keep a refcount on the loop */	4943	/* cleanup watchers should never keep a refcount on the loop */
4239	ev_unref (EV_A);	4944	ev_unref (EV_A);
4240	EV_FREQUENT_CHECK;	4945	EV_FREQUENT_CHECK;
4241	}	4946	}
4242		4947
4243	void	4948	void
4244	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_THROW	4949	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4245	{	4950	{
4246	clear_pending (EV_A_ (W)w);	4951	clear_pending (EV_A_ (W)w);
4247	if (expect_false (!ev_is_active (w)))	4952	if (expect_false (!ev_is_active (w)))
4248	return;	4953	return;
4249		4954
…		…
4263	}	4968	}
4264	#endif	4969	#endif
4265		4970
4266	#if EV_ASYNC_ENABLE	4971	#if EV_ASYNC_ENABLE
4267	void	4972	void
4268	ev_async_start (EV_P_ ev_async *w) EV_THROW	4973	ev_async_start (EV_P_ ev_async *w) EV_NOEXCEPT
4269	{	4974	{
4270	if (expect_false (ev_is_active (w)))	4975	if (expect_false (ev_is_active (w)))
4271	return;	4976	return;
4272		4977
4273	w->sent = 0;	4978	w->sent = 0;
…		…
4275	evpipe_init (EV_A);	4980	evpipe_init (EV_A);
4276		4981
4277	EV_FREQUENT_CHECK;	4982	EV_FREQUENT_CHECK;
4278		4983
4279	ev_start (EV_A_ (W)w, ++asynccnt);	4984	ev_start (EV_A_ (W)w, ++asynccnt);
4280	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, EMPTY2);	4985	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, array_needsize_noinit);
4281	asyncs [asynccnt - 1] = w;	4986	asyncs [asynccnt - 1] = w;
4282		4987
4283	EV_FREQUENT_CHECK;	4988	EV_FREQUENT_CHECK;
4284	}	4989	}
4285		4990
4286	void	4991	void
4287	ev_async_stop (EV_P_ ev_async *w) EV_THROW	4992	ev_async_stop (EV_P_ ev_async *w) EV_NOEXCEPT
4288	{	4993	{
4289	clear_pending (EV_A_ (W)w);	4994	clear_pending (EV_A_ (W)w);
4290	if (expect_false (!ev_is_active (w)))	4995	if (expect_false (!ev_is_active (w)))
4291	return;	4996	return;
4292		4997
…		…
4303		5008
4304	EV_FREQUENT_CHECK;	5009	EV_FREQUENT_CHECK;
4305	}	5010	}
4306		5011
4307	void	5012	void
4308	ev_async_send (EV_P_ ev_async *w) EV_THROW	5013	ev_async_send (EV_P_ ev_async *w) EV_NOEXCEPT
4309	{	5014	{
4310	w->sent = 1;	5015	w->sent = 1;
4311	evpipe_write (EV_A_ &async_pending);	5016	evpipe_write (EV_A_ &async_pending);
4312	}	5017	}
4313	#endif	5018	#endif
…		…
4350		5055
4351	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));	5056	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));
4352	}	5057	}
4353		5058
4354	void	5059	void
4355	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_THROW	5060	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_NOEXCEPT
4356	{	5061	{
4357	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));	5062	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));
4358
4359	if (expect_false (!once))
4360	{
4361	cb (EV_ERROR | EV_READ | EV_WRITE | EV_TIMER, arg);
4362	return;
4363	}
4364		5063
4365	once->cb = cb;	5064	once->cb = cb;
4366	once->arg = arg;	5065	once->arg = arg;
4367		5066
4368	ev_init (&once->io, once_cb_io);	5067	ev_init (&once->io, once_cb_io);
…		…
4381	}	5080	}
4382		5081
4383	/*****************************************************************************/	5082	/*****************************************************************************/
4384		5083
4385	#if EV_WALK_ENABLE	5084	#if EV_WALK_ENABLE
4386	void ecb_cold	5085	ecb_cold
		5086	void
4387	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_THROW	5087	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_NOEXCEPT
4388	{	5088	{
4389	int i, j;	5089	int i, j;
4390	ev_watcher_list *wl, *wn;	5090	ev_watcher_list *wl, *wn;
4391		5091
4392	if (types & (EV_IO | EV_EMBED))	5092	if (types & (EV_IO | EV_EMBED))

Diff Legend

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