ViewVC Help

View File | Revision Log | Show Annotations | Download File

/cvs/libev/ev.c

Comparing libev/ev.c (file contents):
Revision 1.429 by root, Tue May 8 15:50:49 2012 UTC vs.
Revision 1.504 by root, Sun Jul 7 06:00:32 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	# include <winsock2.h>
208	# ifndef EV_SELECT_IS_WINSOCKET	227	# ifndef EV_SELECT_IS_WINSOCKET
209	# define EV_SELECT_IS_WINSOCKET 1	228	# define EV_SELECT_IS_WINSOCKET 1
210	# endif	229	# endif
211	# undef EV_AVOID_STDIO	230	# undef EV_AVOID_STDIO
212	#endif	231	#endif
213
214	/* OS X, in its infinite idiocy, actually HARDCODES
215	* a limit of 1024 into their select. Where people have brains,
216	* OS X engineers apparently have a vacuum. Or maybe they were
217	* ordered to have a vacuum, or they do anything for money.
218	* This might help. Or not.
219	*/
220	#define _DARWIN_UNLIMITED_SELECT 1
221		232
222	/* this block tries to deduce configuration from header-defined symbols and defaults */	233	/* this block tries to deduce configuration from header-defined symbols and defaults */
223		234
224	/* try to deduce the maximum number of signals on this platform */	235	/* try to deduce the maximum number of signals on this platform */
225	#if defined EV_NSIG	236	#if defined EV_NSIG
…		…
241	#elif defined SIGARRAYSIZE	252	#elif defined SIGARRAYSIZE
242	# define EV_NSIG (SIGARRAYSIZE) /* Assume ary[SIGARRAYSIZE] */	253	# define EV_NSIG (SIGARRAYSIZE) /* Assume ary[SIGARRAYSIZE] */
243	#elif defined _sys_nsig	254	#elif defined _sys_nsig
244	# define EV_NSIG (_sys_nsig) /* Solaris 2.5 */	255	# define EV_NSIG (_sys_nsig) /* Solaris 2.5 */
245	#else	256	#else
246	# error "unable to find value for NSIG, please report"	257	# define EV_NSIG (8 * sizeof (sigset_t) + 1)
247	/* to make it compile regardless, just remove the above line, */
248	/* but consider reporting it, too! :) */
249	# define EV_NSIG 65
250	#endif	258	#endif
251		259
252	#ifndef EV_USE_FLOOR	260	#ifndef EV_USE_FLOOR
253	# define EV_USE_FLOOR 0	261	# define EV_USE_FLOOR 0
254	#endif	262	#endif
255		263
256	#ifndef EV_USE_CLOCK_SYSCALL	264	#ifndef EV_USE_CLOCK_SYSCALL
257	# if __linux && __GLIBC__ >= 2	265	# if __linux && __GLIBC__ == 2 && __GLIBC_MINOR__ < 17
258	# define EV_USE_CLOCK_SYSCALL EV_FEATURE_OS	266	# define EV_USE_CLOCK_SYSCALL EV_FEATURE_OS
259	# else	267	# else
260	# define EV_USE_CLOCK_SYSCALL 0	268	# define EV_USE_CLOCK_SYSCALL 0
		269	# endif
		270	#endif
		271
		272	#if !(_POSIX_TIMERS > 0)
		273	# ifndef EV_USE_MONOTONIC
		274	# define EV_USE_MONOTONIC 0
		275	# endif
		276	# ifndef EV_USE_REALTIME
		277	# define EV_USE_REALTIME 0
261	# endif	278	# endif
262	#endif	279	#endif
263		280
264	#ifndef EV_USE_MONOTONIC	281	#ifndef EV_USE_MONOTONIC
265	# if defined _POSIX_MONOTONIC_CLOCK && _POSIX_MONOTONIC_CLOCK >= 0	282	# if defined _POSIX_MONOTONIC_CLOCK && _POSIX_MONOTONIC_CLOCK >= 0
…		…
307		324
308	#ifndef EV_USE_PORT	325	#ifndef EV_USE_PORT
309	# define EV_USE_PORT 0	326	# define EV_USE_PORT 0
310	#endif	327	#endif
311		328
		329	#ifndef EV_USE_LINUXAIO
		330	# if __linux /* libev currently assumes linux/aio_abi.h is always available on linux */
		331	# define EV_USE_LINUXAIO 1
		332	# else
		333	# define EV_USE_LINUXAIO 0
		334	# endif
		335	#endif
		336
		337	#ifndef EV_USE_IOURING
		338	# if __linux
		339	# define EV_USE_IOURING 0
		340	# else
		341	# define EV_USE_IOURING 0
		342	# endif
		343	#endif
		344
312	#ifndef EV_USE_INOTIFY	345	#ifndef EV_USE_INOTIFY
313	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))	346	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))
314	# define EV_USE_INOTIFY EV_FEATURE_OS	347	# define EV_USE_INOTIFY EV_FEATURE_OS
315	# else	348	# else
316	# define EV_USE_INOTIFY 0	349	# define EV_USE_INOTIFY 0
…		…
355	# define EV_USE_4HEAP EV_FEATURE_DATA	388	# define EV_USE_4HEAP EV_FEATURE_DATA
356	#endif	389	#endif
357		390
358	#ifndef EV_HEAP_CACHE_AT	391	#ifndef EV_HEAP_CACHE_AT
359	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA	392	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA
		393	#endif
		394
		395	#ifdef __ANDROID__
		396	/* supposedly, android doesn't typedef fd_mask */
		397	# undef EV_USE_SELECT
		398	# define EV_USE_SELECT 0
		399	/* supposedly, we need to include syscall.h, not sys/syscall.h, so just disable */
		400	# undef EV_USE_CLOCK_SYSCALL
		401	# define EV_USE_CLOCK_SYSCALL 0
		402	#endif
		403
		404	/* aix's poll.h seems to cause lots of trouble */
		405	#ifdef _AIX
		406	/* AIX has a completely broken poll.h header */
		407	# undef EV_USE_POLL
		408	# define EV_USE_POLL 0
360	#endif	409	#endif
361		410
362	/* on linux, we can use a (slow) syscall to avoid a dependency on pthread, */	411	/* on linux, we can use a (slow) syscall to avoid a dependency on pthread, */
363	/* which makes programs even slower. might work on other unices, too. */	412	/* which makes programs even slower. might work on other unices, too. */
364	#if EV_USE_CLOCK_SYSCALL	413	#if EV_USE_CLOCK_SYSCALL
365	# include <sys/syscall.h>	414	# include <sys/syscall.h>
366	# ifdef SYS_clock_gettime	415	# ifdef SYS_clock_gettime
367	# define clock_gettime(id, ts) syscall (SYS_clock_gettime, (id), (ts))	416	# define clock_gettime(id, ts) syscall (SYS_clock_gettime, (id), (ts))
368	# undef EV_USE_MONOTONIC	417	# undef EV_USE_MONOTONIC
369	# define EV_USE_MONOTONIC 1	418	# define EV_USE_MONOTONIC 1
		419	# define EV_NEED_SYSCALL 1
370	# else	420	# else
371	# undef EV_USE_CLOCK_SYSCALL	421	# undef EV_USE_CLOCK_SYSCALL
372	# define EV_USE_CLOCK_SYSCALL 0	422	# define EV_USE_CLOCK_SYSCALL 0
373	# endif	423	# endif
374	#endif	424	#endif
375		425
376	/* this block fixes any misconfiguration where we know we run into trouble otherwise */	426	/* this block fixes any misconfiguration where we know we run into trouble otherwise */
377		427
378	#ifdef _AIX
379	/* AIX has a completely broken poll.h header */
380	# undef EV_USE_POLL
381	# define EV_USE_POLL 0
382	#endif
383
384	#ifndef CLOCK_MONOTONIC	428	#ifndef CLOCK_MONOTONIC
385	# undef EV_USE_MONOTONIC	429	# undef EV_USE_MONOTONIC
386	# define EV_USE_MONOTONIC 0	430	# define EV_USE_MONOTONIC 0
387	#endif	431	#endif
388		432
…		…
398		442
399	#if !EV_USE_NANOSLEEP	443	#if !EV_USE_NANOSLEEP
400	/* hp-ux has it in sys/time.h, which we unconditionally include above */	444	/* hp-ux has it in sys/time.h, which we unconditionally include above */
401	# if !defined _WIN32 && !defined __hpux	445	# if !defined _WIN32 && !defined __hpux
402	# include <sys/select.h>	446	# include <sys/select.h>
		447	# endif
		448	#endif
		449
		450	#if EV_USE_LINUXAIO
		451	# include <sys/syscall.h>
		452	# if SYS_io_getevents && EV_USE_EPOLL /* linuxaio backend requires epoll backend */
		453	# define EV_NEED_SYSCALL 1
		454	# else
		455	# undef EV_USE_LINUXAIO
		456	# define EV_USE_LINUXAIO 0
		457	# endif
		458	#endif
		459
		460	#if EV_USE_IOURING
		461	# include <sys/syscall.h>
		462	# if !SYS_io_uring_setup && __linux && !__alpha
		463	# define SYS_io_uring_setup 425
		464	# define SYS_io_uring_enter 426
		465	# define SYS_io_uring_wregister 427
		466	# endif
		467	# if SYS_io_uring_setup && EV_USE_EPOLL /* iouring backend requires epoll backend */
		468	# define EV_NEED_SYSCALL 1
		469	# else
		470	# undef EV_USE_IOURING
		471	# define EV_USE_IOURING 0
403	# endif	472	# endif
404	#endif	473	#endif
405		474
406	#if EV_USE_INOTIFY	475	#if EV_USE_INOTIFY
407	# include <sys/statfs.h>	476	# include <sys/statfs.h>
…		…
409	/* some very old inotify.h headers don't have IN_DONT_FOLLOW */	478	/* some very old inotify.h headers don't have IN_DONT_FOLLOW */
410	# ifndef IN_DONT_FOLLOW	479	# ifndef IN_DONT_FOLLOW
411	# undef EV_USE_INOTIFY	480	# undef EV_USE_INOTIFY
412	# define EV_USE_INOTIFY 0	481	# define EV_USE_INOTIFY 0
413	# endif	482	# endif
414	#endif
415
416	#if EV_SELECT_IS_WINSOCKET
417	# include <winsock.h>
418	#endif	483	#endif
419		484
420	#if EV_USE_EVENTFD	485	#if EV_USE_EVENTFD
421	/* our minimum requirement is glibc 2.7 which has the stub, but not the header */	486	/* our minimum requirement is glibc 2.7 which has the stub, but not the header */
422	# include <stdint.h>	487	# include <stdint.h>
…		…
453	uint32_t ssi_signo;	518	uint32_t ssi_signo;
454	char pad[128 - sizeof (uint32_t)];	519	char pad[128 - sizeof (uint32_t)];
455	};	520	};
456	#endif	521	#endif
457		522
458	/**/	523	/*****************************************************************************/
459		524
460	#if EV_VERIFY >= 3	525	#if EV_VERIFY >= 3
461	# define EV_FREQUENT_CHECK ev_verify (EV_A)	526	# define EV_FREQUENT_CHECK ev_verify (EV_A)
462	#else	527	#else
463	# define EV_FREQUENT_CHECK do { } while (0)	528	# define EV_FREQUENT_CHECK do { } while (0)
…		…
468	* This value is good at least till the year 4000.	533	* This value is good at least till the year 4000.
469	*/	534	*/
470	#define MIN_INTERVAL 0.0001220703125 /* 1/2**13, good till 4000 */	535	#define MIN_INTERVAL 0.0001220703125 /* 1/2**13, good till 4000 */
471	/*#define MIN_INTERVAL 0.00000095367431640625 /* 1/2**20, good till 2200 */	536	/*#define MIN_INTERVAL 0.00000095367431640625 /* 1/2**20, good till 2200 */
472		537
473	#define MIN_TIMEJUMP 1. /* minimum timejump that gets detected (if monotonic clock available) */	538	#define MIN_TIMEJUMP 1. /* minimum timejump that gets detected (if monotonic clock available) */
474	#define MAX_BLOCKTIME 59.743 /* never wait longer than this time (to detect time jumps) */	539	#define MAX_BLOCKTIME 59.743 /* never wait longer than this time (to detect time jumps) */
		540
		541	/* find a portable timestamp that is "alawys" in the future but fits into time_t.
		542	* this is quite hard, and we are mostly guessing - we handle 32 bit signed/unsigned time_t,
		543	* and sizes large than 32 bit, but and maybe the unlikely loating point time_t */
		544	#define EV_TSTAMP_HUGE \
		545	(sizeof (time_t) >= 8 ? 10000000000000. \
		546	: 0 < (time_t)4294967295 ? 4294967295. \
		547	: 2147483647.) \
475		548
476	#define EV_TV_SET(tv,t) do { tv.tv_sec = (long)t; tv.tv_usec = (long)((t - tv.tv_sec) * 1e6); } while (0)	549	#define EV_TV_SET(tv,t) do { tv.tv_sec = (long)t; tv.tv_usec = (long)((t - tv.tv_sec) * 1e6); } while (0)
477	#define EV_TS_SET(ts,t) do { ts.tv_sec = (long)t; ts.tv_nsec = (long)((t - ts.tv_sec) * 1e9); } while (0)	550	#define EV_TS_SET(ts,t) do { ts.tv_sec = (long)t; ts.tv_nsec = (long)((t - ts.tv_sec) * 1e9); } while (0)
478		551
479	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */	552	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */
480	/* ECB.H BEGIN */	553	/* ECB.H BEGIN */
481	/*	554	/*
482	* libecb - http://software.schmorp.de/pkg/libecb	555	* libecb - http://software.schmorp.de/pkg/libecb
483	*	556	*
484	* Copyright (©) 2009-2012 Marc Alexander Lehmann <libecb@schmorp.de>	557	* Copyright (©) 2009-2015 Marc Alexander Lehmann <libecb@schmorp.de>
485	* Copyright (©) 2011 Emanuele Giaquinta	558	* Copyright (©) 2011 Emanuele Giaquinta
486	* All rights reserved.	559	* All rights reserved.
487	*	560	*
488	* Redistribution and use in source and binary forms, with or without modifica-	561	* Redistribution and use in source and binary forms, with or without modifica-
489	* tion, are permitted provided that the following conditions are met:	562	* tion, are permitted provided that the following conditions are met:
…		…
503	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;	576	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;
504	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,	577	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,
505	* WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING NEGLIGENCE OR OTH-	578	* WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING NEGLIGENCE OR OTH-
506	* ERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED	579	* ERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED
507	* OF THE POSSIBILITY OF SUCH DAMAGE.	580	* OF THE POSSIBILITY OF SUCH DAMAGE.
		581	*
		582	* Alternatively, the contents of this file may be used under the terms of
		583	* the GNU General Public License ("GPL") version 2 or any later version,
		584	* in which case the provisions of the GPL are applicable instead of
		585	* the above. If you wish to allow the use of your version of this file
		586	* only under the terms of the GPL and not to allow others to use your
		587	* version of this file under the BSD license, indicate your decision
		588	* by deleting the provisions above and replace them with the notice
		589	* and other provisions required by the GPL. If you do not delete the
		590	* provisions above, a recipient may use your version of this file under
		591	* either the BSD or the GPL.
508	*/	592	*/
509		593
510	#ifndef ECB_H	594	#ifndef ECB_H
511	#define ECB_H	595	#define ECB_H
		596
		597	/* 16 bits major, 16 bits minor */
		598	#define ECB_VERSION 0x00010006
512		599
513	#ifdef _WIN32	600	#ifdef _WIN32
514	typedef signed char int8_t;	601	typedef signed char int8_t;
515	typedef unsigned char uint8_t;	602	typedef unsigned char uint8_t;
516	typedef signed short int16_t;	603	typedef signed short int16_t;
…		…
522	typedef unsigned long long uint64_t;	609	typedef unsigned long long uint64_t;
523	#else /* _MSC_VER || __BORLANDC__ */	610	#else /* _MSC_VER || __BORLANDC__ */
524	typedef signed __int64 int64_t;	611	typedef signed __int64 int64_t;
525	typedef unsigned __int64 uint64_t;	612	typedef unsigned __int64 uint64_t;
526	#endif	613	#endif
		614	#ifdef _WIN64
		615	#define ECB_PTRSIZE 8
		616	typedef uint64_t uintptr_t;
		617	typedef int64_t intptr_t;
		618	#else
		619	#define ECB_PTRSIZE 4
		620	typedef uint32_t uintptr_t;
		621	typedef int32_t intptr_t;
		622	#endif
527	#else	623	#else
528	#include <inttypes.h>	624	#include <inttypes.h>
		625	#if (defined INTPTR_MAX ? INTPTR_MAX : ULONG_MAX) > 0xffffffffU
		626	#define ECB_PTRSIZE 8
		627	#else
		628	#define ECB_PTRSIZE 4
		629	#endif
		630	#endif
		631
		632	#define ECB_GCC_AMD64 (__amd64 || __amd64__ || __x86_64 || __x86_64__)
		633	#define ECB_MSVC_AMD64 (_M_AMD64 || _M_X64)
		634
		635	/* work around x32 idiocy by defining proper macros */
		636	#if ECB_GCC_AMD64 || ECB_MSVC_AMD64
		637	#if _ILP32
		638	#define ECB_AMD64_X32 1
		639	#else
		640	#define ECB_AMD64 1
		641	#endif
529	#endif	642	#endif
530		643
531	/* many compilers define _GNUC_ to some versions but then only implement	644	/* many compilers define _GNUC_ to some versions but then only implement
532	* what their idiot authors think are the "more important" extensions,	645	* what their idiot authors think are the "more important" extensions,
533	* causing enormous grief in return for some better fake benchmark numbers.	646	* causing enormous grief in return for some better fake benchmark numbers.
534	* or so.	647	* or so.
535	* we try to detect these and simply assume they are not gcc - if they have	648	* we try to detect these and simply assume they are not gcc - if they have
536	* an issue with that they should have done it right in the first place.	649	* an issue with that they should have done it right in the first place.
537	*/	650	*/
538	#ifndef ECB_GCC_VERSION
539	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__	651	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__
540	#define ECB_GCC_VERSION(major,minor) 0	652	#define ECB_GCC_VERSION(major,minor) 0
541	#else	653	#else
542	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))	654	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))
543	#endif	655	#endif
		656
		657	#define ECB_CLANG_VERSION(major,minor) (__clang_major__ > (major) || (__clang_major__ == (major) && __clang_minor__ >= (minor)))
		658
		659	#if __clang__ && defined __has_builtin
		660	#define ECB_CLANG_BUILTIN(x) __has_builtin (x)
		661	#else
		662	#define ECB_CLANG_BUILTIN(x) 0
		663	#endif
		664
		665	#if __clang__ && defined __has_extension
		666	#define ECB_CLANG_EXTENSION(x) __has_extension (x)
		667	#else
		668	#define ECB_CLANG_EXTENSION(x) 0
		669	#endif
		670
		671	#define ECB_CPP (__cplusplus+0)
		672	#define ECB_CPP11 (__cplusplus >= 201103L)
		673	#define ECB_CPP14 (__cplusplus >= 201402L)
		674	#define ECB_CPP17 (__cplusplus >= 201703L)
		675
		676	#if ECB_CPP
		677	#define ECB_C 0
		678	#define ECB_STDC_VERSION 0
		679	#else
		680	#define ECB_C 1
		681	#define ECB_STDC_VERSION __STDC_VERSION__
		682	#endif
		683
		684	#define ECB_C99 (ECB_STDC_VERSION >= 199901L)
		685	#define ECB_C11 (ECB_STDC_VERSION >= 201112L)
		686	#define ECB_C17 (ECB_STDC_VERSION >= 201710L)
		687
		688	#if ECB_CPP
		689	#define ECB_EXTERN_C extern "C"
		690	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {
		691	#define ECB_EXTERN_C_END }
		692	#else
		693	#define ECB_EXTERN_C extern
		694	#define ECB_EXTERN_C_BEG
		695	#define ECB_EXTERN_C_END
544	#endif	696	#endif
545		697
546	/*****************************************************************************/	698	/*****************************************************************************/
547		699
548	/* ECB_NO_THREADS - ecb is not used by multiple threads, ever */	700	/* ECB_NO_THREADS - ecb is not used by multiple threads, ever */
549	/* ECB_NO_SMP - ecb might be used in multiple threads, but only on a single cpu */	701	/* ECB_NO_SMP - ecb might be used in multiple threads, but only on a single cpu */
550		702
551	#if ECB_NO_THREADS	703	#if ECB_NO_THREADS
552	# define ECB_NO_SMP 1	704	#define ECB_NO_SMP 1
553	#endif	705	#endif
554		706
555	#if ECB_NO_THREADS || ECB_NO_SMP	707	#if ECB_NO_SMP
556	#define ECB_MEMORY_FENCE do { } while (0)	708	#define ECB_MEMORY_FENCE do { } while (0)
		709	#endif
		710
		711	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/compiler_ref/compiler_builtins.html */
		712	#if __xlC__ && ECB_CPP
		713	#include <builtins.h>
		714	#endif
		715
		716	#if 1400 <= _MSC_VER
		717	#include <intrin.h> /* fence functions _ReadBarrier, also bit search functions _BitScanReverse */
557	#endif	718	#endif
558		719
559	#ifndef ECB_MEMORY_FENCE	720	#ifndef ECB_MEMORY_FENCE
560	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	721	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
		722	#define ECB_MEMORY_FENCE_RELAXED __asm__ __volatile__ ("" : : : "memory")
561	#if __i386 || __i386__	723	#if __i386 || __i386__
562	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")	724	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")
563	#define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE /* non-lock xchg might be enough */	725	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
564	#define ECB_MEMORY_FENCE_RELEASE do { } while (0) /* unlikely to change in future cpus */	726	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
565	#elif __amd64 || __amd64__ || __x86_64 || __x86_64__	727	#elif ECB_GCC_AMD64
566	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")	728	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")
567	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("lfence" : : : "memory")	729	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
568	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("sfence") /* play safe - not needed in any current cpu */	730	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
569	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__	731	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__
570	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")	732	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")
		733	#elif defined __ARM_ARCH_2__ \
		734	|| defined __ARM_ARCH_3__ || defined __ARM_ARCH_3M__ \
		735	|| defined __ARM_ARCH_4__ || defined __ARM_ARCH_4T__ \
		736	|| defined __ARM_ARCH_5__ || defined __ARM_ARCH_5E__ \
		737	|| defined __ARM_ARCH_5T__ || defined __ARM_ARCH_5TE__ \
		738	|| defined __ARM_ARCH_5TEJ__
		739	/* should not need any, unless running old code on newer cpu - arm doesn't support that */
571	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \	740	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \
572	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__	741	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__ \
		742	|| defined __ARM_ARCH_6T2__
573	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")	743	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")
574	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \	744	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \
575	|| defined __ARM_ARCH_7M__ || defined __ARM_ARCH_7R__	745	|| defined __ARM_ARCH_7R__ || defined __ARM_ARCH_7M__
576	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")	746	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")
577	#elif __sparc || __sparc__	747	#elif __aarch64__
		748	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb ish" : : : "memory")
		749	#elif (__sparc || __sparc__) && !(__sparc_v8__ || defined __sparcv8)
578	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad | " : : : "memory")	750	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")
579	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")	751	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")
580	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")	752	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")
581	#elif defined __s390__ || defined __s390x__	753	#elif defined __s390__ || defined __s390x__
582	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")	754	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")
583	#elif defined __mips__	755	#elif defined __mips__
		756	/* GNU/Linux emulates sync on mips1 architectures, so we force its use */
		757	/* anybody else who still uses mips1 is supposed to send in their version, with detection code. */
584	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")	758	#define ECB_MEMORY_FENCE __asm__ __volatile__ (".set mips2; sync; .set mips0" : : : "memory")
585	#elif defined __alpha__	759	#elif defined __alpha__
586	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mb" : : : "memory")	760	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mb" : : : "memory")
		761	#elif defined __hppa__
		762	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("" : : : "memory")
		763	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")
		764	#elif defined __ia64__
		765	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mf" : : : "memory")
		766	#elif defined __m68k__
		767	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("" : : : "memory")
		768	#elif defined __m88k__
		769	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("tb1 0,%%r0,128" : : : "memory")
		770	#elif defined __sh__
		771	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("" : : : "memory")
587	#endif	772	#endif
588	#endif	773	#endif
589	#endif	774	#endif
590		775
591	#ifndef ECB_MEMORY_FENCE	776	#ifndef ECB_MEMORY_FENCE
		777	#if ECB_GCC_VERSION(4,7)
		778	/* see comment below (stdatomic.h) about the C11 memory model. */
		779	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)
		780	#define ECB_MEMORY_FENCE_ACQUIRE __atomic_thread_fence (__ATOMIC_ACQUIRE)
		781	#define ECB_MEMORY_FENCE_RELEASE __atomic_thread_fence (__ATOMIC_RELEASE)
		782	#define ECB_MEMORY_FENCE_RELAXED __atomic_thread_fence (__ATOMIC_RELAXED)
		783
		784	#elif ECB_CLANG_EXTENSION(c_atomic)
		785	/* see comment below (stdatomic.h) about the C11 memory model. */
		786	#define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)
		787	#define ECB_MEMORY_FENCE_ACQUIRE __c11_atomic_thread_fence (__ATOMIC_ACQUIRE)
		788	#define ECB_MEMORY_FENCE_RELEASE __c11_atomic_thread_fence (__ATOMIC_RELEASE)
		789	#define ECB_MEMORY_FENCE_RELAXED __c11_atomic_thread_fence (__ATOMIC_RELAXED)
		790
592	#if ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__	791	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__
593	#define ECB_MEMORY_FENCE __sync_synchronize ()	792	#define ECB_MEMORY_FENCE __sync_synchronize ()
594	/*#define ECB_MEMORY_FENCE_ACQUIRE ({ char dummy = 0; __sync_lock_test_and_set (&dummy, 1); }) */	793	#elif _MSC_VER >= 1500 /* VC++ 2008 */
595	/*#define ECB_MEMORY_FENCE_RELEASE ({ char dummy = 1; __sync_lock_release (&dummy ); }) */	794	/* apparently, microsoft broke all the memory barrier stuff in Visual Studio 2008... */
		795	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)
		796	#define ECB_MEMORY_FENCE _ReadWriteBarrier (); MemoryBarrier()
		797	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier (); MemoryBarrier() /* according to msdn, _ReadBarrier is not a load fence */
		798	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier (); MemoryBarrier()
596	#elif _MSC_VER >= 1400 /* VC++ 2005 */	799	#elif _MSC_VER >= 1400 /* VC++ 2005 */
597	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)	800	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)
598	#define ECB_MEMORY_FENCE _ReadWriteBarrier ()	801	#define ECB_MEMORY_FENCE _ReadWriteBarrier ()
599	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier () /* according to msdn, _ReadBarrier is not a load fence */	802	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier () /* according to msdn, _ReadBarrier is not a load fence */
600	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier ()	803	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier ()
601	#elif defined _WIN32	804	#elif defined _WIN32
602	#include <WinNT.h>	805	#include <WinNT.h>
603	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */	806	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */
604	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	807	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
605	#include <mbarrier.h>	808	#include <mbarrier.h>
606	#define ECB_MEMORY_FENCE __machine_rw_barrier ()	809	#define ECB_MEMORY_FENCE __machine_rw_barrier ()
607	#define ECB_MEMORY_FENCE_ACQUIRE __machine_r_barrier ()	810	#define ECB_MEMORY_FENCE_ACQUIRE __machine_acq_barrier ()
608	#define ECB_MEMORY_FENCE_RELEASE __machine_w_barrier ()	811	#define ECB_MEMORY_FENCE_RELEASE __machine_rel_barrier ()
		812	#define ECB_MEMORY_FENCE_RELAXED __compiler_barrier ()
609	#elif __xlC__	813	#elif __xlC__
610	#define ECB_MEMORY_FENCE __sync ()	814	#define ECB_MEMORY_FENCE __sync ()
		815	#endif
		816	#endif
		817
		818	#ifndef ECB_MEMORY_FENCE
		819	#if ECB_C11 && !defined __STDC_NO_ATOMICS__
		820	/* we assume that these memory fences work on all variables/all memory accesses, */
		821	/* not just C11 atomics and atomic accesses */
		822	#include <stdatomic.h>
		823	#define ECB_MEMORY_FENCE atomic_thread_fence (memory_order_seq_cst)
		824	#define ECB_MEMORY_FENCE_ACQUIRE atomic_thread_fence (memory_order_acquire)
		825	#define ECB_MEMORY_FENCE_RELEASE atomic_thread_fence (memory_order_release)
611	#endif	826	#endif
612	#endif	827	#endif
613		828
614	#ifndef ECB_MEMORY_FENCE	829	#ifndef ECB_MEMORY_FENCE
615	#if !ECB_AVOID_PTHREADS	830	#if !ECB_AVOID_PTHREADS
…		…
635		850
636	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE	851	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE
637	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	852	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
638	#endif	853	#endif
639		854
		855	#if !defined ECB_MEMORY_FENCE_RELAXED && defined ECB_MEMORY_FENCE
		856	#define ECB_MEMORY_FENCE_RELAXED ECB_MEMORY_FENCE /* very heavy-handed */
		857	#endif
		858
640	/*****************************************************************************/	859	/*****************************************************************************/
641		860
642	#define ECB_C99 (__STDC_VERSION__ >= 199901L)	861	#if ECB_CPP
643
644	#if __cplusplus
645	#define ecb_inline static inline	862	#define ecb_inline static inline
646	#elif ECB_GCC_VERSION(2,5)	863	#elif ECB_GCC_VERSION(2,5)
647	#define ecb_inline static __inline__	864	#define ecb_inline static __inline__
648	#elif ECB_C99	865	#elif ECB_C99
649	#define ecb_inline static inline	866	#define ecb_inline static inline
…		…
663		880
664	#define ECB_CONCAT_(a, b) a ## b	881	#define ECB_CONCAT_(a, b) a ## b
665	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)	882	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)
666	#define ECB_STRINGIFY_(a) # a	883	#define ECB_STRINGIFY_(a) # a
667	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)	884	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)
		885	#define ECB_STRINGIFY_EXPR(expr) ((expr), ECB_STRINGIFY_ (expr))
668		886
669	#define ecb_function_ ecb_inline	887	#define ecb_function_ ecb_inline
670		888
671	#if ECB_GCC_VERSION(3,1)	889	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_VERSION(2,8)
672	#define ecb_attribute(attrlist) __attribute__(attrlist)	890	#define ecb_attribute(attrlist) __attribute__ (attrlist)
		891	#else
		892	#define ecb_attribute(attrlist)
		893	#endif
		894
		895	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_constant_p)
673	#define ecb_is_constant(expr) __builtin_constant_p (expr)	896	#define ecb_is_constant(expr) __builtin_constant_p (expr)
		897	#else
		898	/* possible C11 impl for integral types
		899	typedef struct ecb_is_constant_struct ecb_is_constant_struct;
		900	#define ecb_is_constant(expr) _Generic ((1 ? (struct ecb_is_constant_struct *)0 : (void *)((expr) - (expr)), ecb_is_constant_struct *: 0, default: 1)) */
		901
		902	#define ecb_is_constant(expr) 0
		903	#endif
		904
		905	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_expect)
674	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))	906	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))
		907	#else
		908	#define ecb_expect(expr,value) (expr)
		909	#endif
		910
		911	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_prefetch)
675	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)	912	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)
676	#else	913	#else
677	#define ecb_attribute(attrlist)
678	#define ecb_is_constant(expr) 0
679	#define ecb_expect(expr,value) (expr)
680	#define ecb_prefetch(addr,rw,locality)	914	#define ecb_prefetch(addr,rw,locality)
681	#endif	915	#endif
682		916
683	/* no emulation for ecb_decltype */	917	/* no emulation for ecb_decltype */
684	#if ECB_GCC_VERSION(4,5)	918	#if ECB_CPP11
		919	// older implementations might have problems with decltype(x)::type, work around it
		920	template<class T> struct ecb_decltype_t { typedef T type; };
685	#define ecb_decltype(x) __decltype(x)	921	#define ecb_decltype(x) ecb_decltype_t<decltype (x)>::type
686	#elif ECB_GCC_VERSION(3,0)	922	#elif ECB_GCC_VERSION(3,0) || ECB_CLANG_VERSION(2,8)
687	#define ecb_decltype(x) __typeof(x)	923	#define ecb_decltype(x) __typeof__ (x)
688	#endif	924	#endif
689		925
		926	#if _MSC_VER >= 1300
		927	#define ecb_deprecated __declspec (deprecated)
		928	#else
		929	#define ecb_deprecated ecb_attribute ((__deprecated__))
		930	#endif
		931
		932	#if _MSC_VER >= 1500
		933	#define ecb_deprecated_message(msg) __declspec (deprecated (msg))
		934	#elif ECB_GCC_VERSION(4,5)
		935	#define ecb_deprecated_message(msg) ecb_attribute ((__deprecated__ (msg))
		936	#else
		937	#define ecb_deprecated_message(msg) ecb_deprecated
		938	#endif
		939
		940	#if _MSC_VER >= 1400
		941	#define ecb_noinline __declspec (noinline)
		942	#else
690	#define ecb_noinline ecb_attribute ((__noinline__))	943	#define ecb_noinline ecb_attribute ((__noinline__))
691	#define ecb_noreturn ecb_attribute ((__noreturn__))	944	#endif
		945
692	#define ecb_unused ecb_attribute ((__unused__))	946	#define ecb_unused ecb_attribute ((__unused__))
693	#define ecb_const ecb_attribute ((__const__))	947	#define ecb_const ecb_attribute ((__const__))
694	#define ecb_pure ecb_attribute ((__pure__))	948	#define ecb_pure ecb_attribute ((__pure__))
		949
		950	#if ECB_C11 || __IBMC_NORETURN
		951	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/language_ref/noreturn.html */
		952	#define ecb_noreturn _Noreturn
		953	#elif ECB_CPP11
		954	#define ecb_noreturn [[noreturn]]
		955	#elif _MSC_VER >= 1200
		956	/* http://msdn.microsoft.com/en-us/library/k6ktzx3s.aspx */
		957	#define ecb_noreturn __declspec (noreturn)
		958	#else
		959	#define ecb_noreturn ecb_attribute ((__noreturn__))
		960	#endif
695		961
696	#if ECB_GCC_VERSION(4,3)	962	#if ECB_GCC_VERSION(4,3)
697	#define ecb_artificial ecb_attribute ((__artificial__))	963	#define ecb_artificial ecb_attribute ((__artificial__))
698	#define ecb_hot ecb_attribute ((__hot__))	964	#define ecb_hot ecb_attribute ((__hot__))
699	#define ecb_cold ecb_attribute ((__cold__))	965	#define ecb_cold ecb_attribute ((__cold__))
…		…
711	/* for compatibility to the rest of the world */	977	/* for compatibility to the rest of the world */
712	#define ecb_likely(expr) ecb_expect_true (expr)	978	#define ecb_likely(expr) ecb_expect_true (expr)
713	#define ecb_unlikely(expr) ecb_expect_false (expr)	979	#define ecb_unlikely(expr) ecb_expect_false (expr)
714		980
715	/* count trailing zero bits and count # of one bits */	981	/* count trailing zero bits and count # of one bits */
716	#if ECB_GCC_VERSION(3,4)	982	#if ECB_GCC_VERSION(3,4) \
		983	|| (ECB_CLANG_BUILTIN(__builtin_clz) && ECB_CLANG_BUILTIN(__builtin_clzll) \
		984	&& ECB_CLANG_BUILTIN(__builtin_ctz) && ECB_CLANG_BUILTIN(__builtin_ctzll) \
		985	&& ECB_CLANG_BUILTIN(__builtin_popcount))
717	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */	986	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */
718	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)	987	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)
719	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)	988	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)
720	#define ecb_ctz32(x) __builtin_ctz (x)	989	#define ecb_ctz32(x) __builtin_ctz (x)
721	#define ecb_ctz64(x) __builtin_ctzll (x)	990	#define ecb_ctz64(x) __builtin_ctzll (x)
722	#define ecb_popcount32(x) __builtin_popcount (x)	991	#define ecb_popcount32(x) __builtin_popcount (x)
723	/* no popcountll */	992	/* no popcountll */
724	#else	993	#else
725	ecb_function_ int ecb_ctz32 (uint32_t x) ecb_const;	994	ecb_function_ ecb_const int ecb_ctz32 (uint32_t x);
726	ecb_function_ int	995	ecb_function_ ecb_const int
727	ecb_ctz32 (uint32_t x)	996	ecb_ctz32 (uint32_t x)
728	{	997	{
		998	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		999	unsigned long r;
		1000	_BitScanForward (&r, x);
		1001	return (int)r;
		1002	#else
729	int r = 0;	1003	int r = 0;
730		1004
731	x &= ~x + 1; /* this isolates the lowest bit */	1005	x &= ~x + 1; /* this isolates the lowest bit */
732		1006
733	#if ECB_branchless_on_i386	1007	#if ECB_branchless_on_i386
…		…
743	if (x & 0xff00ff00) r += 8;	1017	if (x & 0xff00ff00) r += 8;
744	if (x & 0xffff0000) r += 16;	1018	if (x & 0xffff0000) r += 16;
745	#endif	1019	#endif
746		1020
747	return r;	1021	return r;
		1022	#endif
748	}	1023	}
749		1024
750	ecb_function_ int ecb_ctz64 (uint64_t x) ecb_const;	1025	ecb_function_ ecb_const int ecb_ctz64 (uint64_t x);
751	ecb_function_ int	1026	ecb_function_ ecb_const int
752	ecb_ctz64 (uint64_t x)	1027	ecb_ctz64 (uint64_t x)
753	{	1028	{
		1029	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1030	unsigned long r;
		1031	_BitScanForward64 (&r, x);
		1032	return (int)r;
		1033	#else
754	int shift = x & 0xffffffffU ? 0 : 32;	1034	int shift = x & 0xffffffff ? 0 : 32;
755	return ecb_ctz32 (x >> shift) + shift;	1035	return ecb_ctz32 (x >> shift) + shift;
		1036	#endif
756	}	1037	}
757		1038
758	ecb_function_ int ecb_popcount32 (uint32_t x) ecb_const;	1039	ecb_function_ ecb_const int ecb_popcount32 (uint32_t x);
759	ecb_function_ int	1040	ecb_function_ ecb_const int
760	ecb_popcount32 (uint32_t x)	1041	ecb_popcount32 (uint32_t x)
761	{	1042	{
762	x -= (x >> 1) & 0x55555555;	1043	x -= (x >> 1) & 0x55555555;
763	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);	1044	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);
764	x = ((x >> 4) + x) & 0x0f0f0f0f;	1045	x = ((x >> 4) + x) & 0x0f0f0f0f;
765	x *= 0x01010101;	1046	x *= 0x01010101;
766		1047
767	return x >> 24;	1048	return x >> 24;
768	}	1049	}
769		1050
770	ecb_function_ int ecb_ld32 (uint32_t x) ecb_const;	1051	ecb_function_ ecb_const int ecb_ld32 (uint32_t x);
771	ecb_function_ int ecb_ld32 (uint32_t x)	1052	ecb_function_ ecb_const int ecb_ld32 (uint32_t x)
772	{	1053	{
		1054	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		1055	unsigned long r;
		1056	_BitScanReverse (&r, x);
		1057	return (int)r;
		1058	#else
773	int r = 0;	1059	int r = 0;
774		1060
775	if (x >> 16) { x >>= 16; r += 16; }	1061	if (x >> 16) { x >>= 16; r += 16; }
776	if (x >> 8) { x >>= 8; r += 8; }	1062	if (x >> 8) { x >>= 8; r += 8; }
777	if (x >> 4) { x >>= 4; r += 4; }	1063	if (x >> 4) { x >>= 4; r += 4; }
778	if (x >> 2) { x >>= 2; r += 2; }	1064	if (x >> 2) { x >>= 2; r += 2; }
779	if (x >> 1) { r += 1; }	1065	if (x >> 1) { r += 1; }
780		1066
781	return r;	1067	return r;
		1068	#endif
782	}	1069	}
783		1070
784	ecb_function_ int ecb_ld64 (uint64_t x) ecb_const;	1071	ecb_function_ ecb_const int ecb_ld64 (uint64_t x);
785	ecb_function_ int ecb_ld64 (uint64_t x)	1072	ecb_function_ ecb_const int ecb_ld64 (uint64_t x)
786	{	1073	{
		1074	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1075	unsigned long r;
		1076	_BitScanReverse64 (&r, x);
		1077	return (int)r;
		1078	#else
787	int r = 0;	1079	int r = 0;
788		1080
789	if (x >> 32) { x >>= 32; r += 32; }	1081	if (x >> 32) { x >>= 32; r += 32; }
790		1082
791	return r + ecb_ld32 (x);	1083	return r + ecb_ld32 (x);
		1084	#endif
792	}	1085	}
793	#endif	1086	#endif
794		1087
		1088	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x);
		1089	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x) { return !(x & (x - 1)); }
		1090	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x);
		1091	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x) { return !(x & (x - 1)); }
		1092
795	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x) ecb_const;	1093	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x);
796	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x)	1094	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x)
797	{	1095	{
798	return ( (x * 0x0802U & 0x22110U)	1096	return ( (x * 0x0802U & 0x22110U)
799	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;	1097	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;
800	}	1098	}
801		1099
802	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x) ecb_const;	1100	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x);
803	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x)	1101	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x)
804	{	1102	{
805	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);	1103	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);
806	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);	1104	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);
807	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);	1105	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);
808	x = ( x >> 8 ) | ( x << 8);	1106	x = ( x >> 8 ) | ( x << 8);
809		1107
810	return x;	1108	return x;
811	}	1109	}
812		1110
813	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x) ecb_const;	1111	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x);
814	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x)	1112	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x)
815	{	1113	{
816	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);	1114	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);
817	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);	1115	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);
818	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);	1116	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);
819	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);	1117	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);
…		…
822	return x;	1120	return x;
823	}	1121	}
824		1122
825	/* popcount64 is only available on 64 bit cpus as gcc builtin */	1123	/* popcount64 is only available on 64 bit cpus as gcc builtin */
826	/* so for this version we are lazy */	1124	/* so for this version we are lazy */
827	ecb_function_ int ecb_popcount64 (uint64_t x) ecb_const;	1125	ecb_function_ ecb_const int ecb_popcount64 (uint64_t x);
828	ecb_function_ int	1126	ecb_function_ ecb_const int
829	ecb_popcount64 (uint64_t x)	1127	ecb_popcount64 (uint64_t x)
830	{	1128	{
831	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);	1129	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);
832	}	1130	}
833		1131
834	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) ecb_const;	1132	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count);
835	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) ecb_const;	1133	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count);
836	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) ecb_const;	1134	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count);
837	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) ecb_const;	1135	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count);
838	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) ecb_const;	1136	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count);
839	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) ecb_const;	1137	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count);
840	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) ecb_const;	1138	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count);
841	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) ecb_const;	1139	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count);
842		1140
843	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }	1141	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }
844	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }	1142	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }
845	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }	1143	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }
846	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }	1144	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }
847	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }	1145	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }
848	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }	1146	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }
849	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }	1147	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }
850	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }	1148	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }
851		1149
852	#if ECB_GCC_VERSION(4,3)	1150	#if ECB_GCC_VERSION(4,3) || (ECB_CLANG_BUILTIN(__builtin_bswap32) && ECB_CLANG_BUILTIN(__builtin_bswap64))
		1151	#if ECB_GCC_VERSION(4,8) || ECB_CLANG_BUILTIN(__builtin_bswap16)
		1152	#define ecb_bswap16(x) __builtin_bswap16 (x)
		1153	#else
853	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)	1154	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)
		1155	#endif
854	#define ecb_bswap32(x) __builtin_bswap32 (x)	1156	#define ecb_bswap32(x) __builtin_bswap32 (x)
855	#define ecb_bswap64(x) __builtin_bswap64 (x)	1157	#define ecb_bswap64(x) __builtin_bswap64 (x)
		1158	#elif _MSC_VER
		1159	#include <stdlib.h>
		1160	#define ecb_bswap16(x) ((uint16_t)_byteswap_ushort ((uint16_t)(x)))
		1161	#define ecb_bswap32(x) ((uint32_t)_byteswap_ulong ((uint32_t)(x)))
		1162	#define ecb_bswap64(x) ((uint64_t)_byteswap_uint64 ((uint64_t)(x)))
856	#else	1163	#else
857	ecb_function_ uint16_t ecb_bswap16 (uint16_t x) ecb_const;	1164	ecb_function_ ecb_const uint16_t ecb_bswap16 (uint16_t x);
858	ecb_function_ uint16_t	1165	ecb_function_ ecb_const uint16_t
859	ecb_bswap16 (uint16_t x)	1166	ecb_bswap16 (uint16_t x)
860	{	1167	{
861	return ecb_rotl16 (x, 8);	1168	return ecb_rotl16 (x, 8);
862	}	1169	}
863		1170
864	ecb_function_ uint32_t ecb_bswap32 (uint32_t x) ecb_const;	1171	ecb_function_ ecb_const uint32_t ecb_bswap32 (uint32_t x);
865	ecb_function_ uint32_t	1172	ecb_function_ ecb_const uint32_t
866	ecb_bswap32 (uint32_t x)	1173	ecb_bswap32 (uint32_t x)
867	{	1174	{
868	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);	1175	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);
869	}	1176	}
870		1177
871	ecb_function_ uint64_t ecb_bswap64 (uint64_t x) ecb_const;	1178	ecb_function_ ecb_const uint64_t ecb_bswap64 (uint64_t x);
872	ecb_function_ uint64_t	1179	ecb_function_ ecb_const uint64_t
873	ecb_bswap64 (uint64_t x)	1180	ecb_bswap64 (uint64_t x)
874	{	1181	{
875	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);	1182	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);
876	}	1183	}
877	#endif	1184	#endif
878		1185
879	#if ECB_GCC_VERSION(4,5)	1186	#if ECB_GCC_VERSION(4,5) || ECB_CLANG_BUILTIN(__builtin_unreachable)
880	#define ecb_unreachable() __builtin_unreachable ()	1187	#define ecb_unreachable() __builtin_unreachable ()
881	#else	1188	#else
882	/* this seems to work fine, but gcc always emits a warning for it :/ */	1189	/* this seems to work fine, but gcc always emits a warning for it :/ */
883	ecb_inline void ecb_unreachable (void) ecb_noreturn;	1190	ecb_inline ecb_noreturn void ecb_unreachable (void);
884	ecb_inline void ecb_unreachable (void) { }	1191	ecb_inline ecb_noreturn void ecb_unreachable (void) { }
885	#endif	1192	#endif
886		1193
887	/* try to tell the compiler that some condition is definitely true */	1194	/* try to tell the compiler that some condition is definitely true */
888	#define ecb_assume(cond) do { if (!(cond)) ecb_unreachable (); } while (0)	1195	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0
889		1196
890	ecb_inline unsigned char ecb_byteorder_helper (void) ecb_const;	1197	ecb_inline ecb_const uint32_t ecb_byteorder_helper (void);
891	ecb_inline unsigned char	1198	ecb_inline ecb_const uint32_t
892	ecb_byteorder_helper (void)	1199	ecb_byteorder_helper (void)
893	{	1200	{
894	const uint32_t u = 0x11223344;	1201	/* the union code still generates code under pressure in gcc, */
895	return *(unsigned char *)&u;	1202	/* but less than using pointers, and always seems to */
		1203	/* successfully return a constant. */
		1204	/* the reason why we have this horrible preprocessor mess */
		1205	/* is to avoid it in all cases, at least on common architectures */
		1206	/* or when using a recent enough gcc version (>= 4.6) */
		1207	#if (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_LITTLE_ENDIAN__) \
		1208	|| ((__i386 || __i386__ || _M_IX86 || ECB_GCC_AMD64 || ECB_MSVC_AMD64) && !__VOS__)
		1209	#define ECB_LITTLE_ENDIAN 1
		1210	return 0x44332211;
		1211	#elif (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__) \
		1212	|| ((__AARCH64EB__ || __MIPSEB__ || __ARMEB__) && !__VOS__)
		1213	#define ECB_BIG_ENDIAN 1
		1214	return 0x11223344;
		1215	#else
		1216	union
		1217	{
		1218	uint8_t c[4];
		1219	uint32_t u;
		1220	} u = { 0x11, 0x22, 0x33, 0x44 };
		1221	return u.u;
		1222	#endif
896	}	1223	}
897		1224
898	ecb_inline ecb_bool ecb_big_endian (void) ecb_const;	1225	ecb_inline ecb_const ecb_bool ecb_big_endian (void);
899	ecb_inline ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11; }	1226	ecb_inline ecb_const ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11223344; }
900	ecb_inline ecb_bool ecb_little_endian (void) ecb_const;	1227	ecb_inline ecb_const ecb_bool ecb_little_endian (void);
901	ecb_inline ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44; }	1228	ecb_inline ecb_const ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44332211; }
902		1229
903	#if ECB_GCC_VERSION(3,0) || ECB_C99	1230	#if ECB_GCC_VERSION(3,0) || ECB_C99
904	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))	1231	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))
905	#else	1232	#else
906	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))	1233	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))
907	#endif	1234	#endif
908		1235
909	#if __cplusplus	1236	#if ECB_CPP
910	template<typename T>	1237	template<typename T>
911	static inline T ecb_div_rd (T val, T div)	1238	static inline T ecb_div_rd (T val, T div)
912	{	1239	{
913	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;	1240	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;
914	}	1241	}
…		…
931	}	1258	}
932	#else	1259	#else
933	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))	1260	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))
934	#endif	1261	#endif
935		1262
		1263	ecb_function_ ecb_const uint32_t ecb_binary16_to_binary32 (uint32_t x);
		1264	ecb_function_ ecb_const uint32_t
		1265	ecb_binary16_to_binary32 (uint32_t x)
		1266	{
		1267	unsigned int s = (x & 0x8000) << (31 - 15);
		1268	int e = (x >> 10) & 0x001f;
		1269	unsigned int m = x & 0x03ff;
		1270
		1271	if (ecb_expect_false (e == 31))
		1272	/* infinity or NaN */
		1273	e = 255 - (127 - 15);
		1274	else if (ecb_expect_false (!e))
		1275	{
		1276	if (ecb_expect_true (!m))
		1277	/* zero, handled by code below by forcing e to 0 */
		1278	e = 0 - (127 - 15);
		1279	else
		1280	{
		1281	/* subnormal, renormalise */
		1282	unsigned int s = 10 - ecb_ld32 (m);
		1283
		1284	m = (m << s) & 0x3ff; /* mask implicit bit */
		1285	e -= s - 1;
		1286	}
		1287	}
		1288
		1289	/* e and m now are normalised, or zero, (or inf or nan) */
		1290	e += 127 - 15;
		1291
		1292	return s | (e << 23) | (m << (23 - 10));
		1293	}
		1294
		1295	ecb_function_ ecb_const uint16_t ecb_binary32_to_binary16 (uint32_t x);
		1296	ecb_function_ ecb_const uint16_t
		1297	ecb_binary32_to_binary16 (uint32_t x)
		1298	{
		1299	unsigned int s = (x >> 16) & 0x00008000; /* sign bit, the easy part */
		1300	unsigned int e = ((x >> 23) & 0x000000ff) - (127 - 15); /* the desired exponent */
		1301	unsigned int m = x & 0x007fffff;
		1302
		1303	x &= 0x7fffffff;
		1304
		1305	/* if it's within range of binary16 normals, use fast path */
		1306	if (ecb_expect_true (0x38800000 <= x && x <= 0x477fefff))
		1307	{
		1308	/* mantissa round-to-even */
		1309	m += 0x00000fff + ((m >> (23 - 10)) & 1);
		1310
		1311	/* handle overflow */
		1312	if (ecb_expect_false (m >= 0x00800000))
		1313	{
		1314	m >>= 1;
		1315	e += 1;
		1316	}
		1317
		1318	return s | (e << 10) | (m >> (23 - 10));
		1319	}
		1320
		1321	/* handle large numbers and infinity */
		1322	if (ecb_expect_true (0x477fefff < x && x <= 0x7f800000))
		1323	return s | 0x7c00;
		1324
		1325	/* handle zero, subnormals and small numbers */
		1326	if (ecb_expect_true (x < 0x38800000))
		1327	{
		1328	/* zero */
		1329	if (ecb_expect_true (!x))
		1330	return s;
		1331
		1332	/* handle subnormals */
		1333
		1334	/* too small, will be zero */
		1335	if (e < (14 - 24)) /* might not be sharp, but is good enough */
		1336	return s;
		1337
		1338	m |= 0x00800000; /* make implicit bit explicit */
		1339
		1340	/* very tricky - we need to round to the nearest e (+10) bit value */
		1341	{
		1342	unsigned int bits = 14 - e;
		1343	unsigned int half = (1 << (bits - 1)) - 1;
		1344	unsigned int even = (m >> bits) & 1;
		1345
		1346	/* if this overflows, we will end up with a normalised number */
		1347	m = (m + half + even) >> bits;
		1348	}
		1349
		1350	return s | m;
		1351	}
		1352
		1353	/* handle NaNs, preserve leftmost nan bits, but make sure we don't turn them into infinities */
		1354	m >>= 13;
		1355
		1356	return s | 0x7c00 | m | !m;
		1357	}
		1358
		1359	/*******************************************************************************/
		1360	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */
		1361
		1362	/* basically, everything uses "ieee pure-endian" floating point numbers */
		1363	/* the only noteworthy exception is ancient armle, which uses order 43218765 */
		1364	#if 0 \
		1365	|| __i386 || __i386__ \
		1366	|| ECB_GCC_AMD64 \
		1367	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \
		1368	|| defined __s390__ || defined __s390x__ \
		1369	|| defined __mips__ \
		1370	|| defined __alpha__ \
		1371	|| defined __hppa__ \
		1372	|| defined __ia64__ \
		1373	|| defined __m68k__ \
		1374	|| defined __m88k__ \
		1375	|| defined __sh__ \
		1376	|| defined _M_IX86 || defined ECB_MSVC_AMD64 || defined _M_IA64 \
		1377	|| (defined __arm__ && (defined __ARM_EABI__ || defined __EABI__ || defined __VFP_FP__ || defined _WIN32_WCE || defined __ANDROID__)) \
		1378	|| defined __aarch64__
		1379	#define ECB_STDFP 1
		1380	#include <string.h> /* for memcpy */
		1381	#else
		1382	#define ECB_STDFP 0
		1383	#endif
		1384
		1385	#ifndef ECB_NO_LIBM
		1386
		1387	#include <math.h> /* for frexp*, ldexp*, INFINITY, NAN */
		1388
		1389	/* only the oldest of old doesn't have this one. solaris. */
		1390	#ifdef INFINITY
		1391	#define ECB_INFINITY INFINITY
		1392	#else
		1393	#define ECB_INFINITY HUGE_VAL
		1394	#endif
		1395
		1396	#ifdef NAN
		1397	#define ECB_NAN NAN
		1398	#else
		1399	#define ECB_NAN ECB_INFINITY
		1400	#endif
		1401
		1402	#if ECB_C99 || _XOPEN_VERSION >= 600 || _POSIX_VERSION >= 200112L
		1403	#define ecb_ldexpf(x,e) ldexpf ((x), (e))
		1404	#define ecb_frexpf(x,e) frexpf ((x), (e))
		1405	#else
		1406	#define ecb_ldexpf(x,e) (float) ldexp ((double) (x), (e))
		1407	#define ecb_frexpf(x,e) (float) frexp ((double) (x), (e))
		1408	#endif
		1409
		1410	/* convert a float to ieee single/binary32 */
		1411	ecb_function_ ecb_const uint32_t ecb_float_to_binary32 (float x);
		1412	ecb_function_ ecb_const uint32_t
		1413	ecb_float_to_binary32 (float x)
		1414	{
		1415	uint32_t r;
		1416
		1417	#if ECB_STDFP
		1418	memcpy (&r, &x, 4);
		1419	#else
		1420	/* slow emulation, works for anything but -0 */
		1421	uint32_t m;
		1422	int e;
		1423
		1424	if (x == 0e0f ) return 0x00000000U;
		1425	if (x > +3.40282346638528860e+38f) return 0x7f800000U;
		1426	if (x < -3.40282346638528860e+38f) return 0xff800000U;
		1427	if (x != x ) return 0x7fbfffffU;
		1428
		1429	m = ecb_frexpf (x, &e) * 0x1000000U;
		1430
		1431	r = m & 0x80000000U;
		1432
		1433	if (r)
		1434	m = -m;
		1435
		1436	if (e <= -126)
		1437	{
		1438	m &= 0xffffffU;
		1439	m >>= (-125 - e);
		1440	e = -126;
		1441	}
		1442
		1443	r |= (e + 126) << 23;
		1444	r |= m & 0x7fffffU;
		1445	#endif
		1446
		1447	return r;
		1448	}
		1449
		1450	/* converts an ieee single/binary32 to a float */
		1451	ecb_function_ ecb_const float ecb_binary32_to_float (uint32_t x);
		1452	ecb_function_ ecb_const float
		1453	ecb_binary32_to_float (uint32_t x)
		1454	{
		1455	float r;
		1456
		1457	#if ECB_STDFP
		1458	memcpy (&r, &x, 4);
		1459	#else
		1460	/* emulation, only works for normals and subnormals and +0 */
		1461	int neg = x >> 31;
		1462	int e = (x >> 23) & 0xffU;
		1463
		1464	x &= 0x7fffffU;
		1465
		1466	if (e)
		1467	x |= 0x800000U;
		1468	else
		1469	e = 1;
		1470
		1471	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */
		1472	r = ecb_ldexpf (x * (0.5f / 0x800000U), e - 126);
		1473
		1474	r = neg ? -r : r;
		1475	#endif
		1476
		1477	return r;
		1478	}
		1479
		1480	/* convert a double to ieee double/binary64 */
		1481	ecb_function_ ecb_const uint64_t ecb_double_to_binary64 (double x);
		1482	ecb_function_ ecb_const uint64_t
		1483	ecb_double_to_binary64 (double x)
		1484	{
		1485	uint64_t r;
		1486
		1487	#if ECB_STDFP
		1488	memcpy (&r, &x, 8);
		1489	#else
		1490	/* slow emulation, works for anything but -0 */
		1491	uint64_t m;
		1492	int e;
		1493
		1494	if (x == 0e0 ) return 0x0000000000000000U;
		1495	if (x > +1.79769313486231470e+308) return 0x7ff0000000000000U;
		1496	if (x < -1.79769313486231470e+308) return 0xfff0000000000000U;
		1497	if (x != x ) return 0X7ff7ffffffffffffU;
		1498
		1499	m = frexp (x, &e) * 0x20000000000000U;
		1500
		1501	r = m & 0x8000000000000000;;
		1502
		1503	if (r)
		1504	m = -m;
		1505
		1506	if (e <= -1022)
		1507	{
		1508	m &= 0x1fffffffffffffU;
		1509	m >>= (-1021 - e);
		1510	e = -1022;
		1511	}
		1512
		1513	r |= ((uint64_t)(e + 1022)) << 52;
		1514	r |= m & 0xfffffffffffffU;
		1515	#endif
		1516
		1517	return r;
		1518	}
		1519
		1520	/* converts an ieee double/binary64 to a double */
		1521	ecb_function_ ecb_const double ecb_binary64_to_double (uint64_t x);
		1522	ecb_function_ ecb_const double
		1523	ecb_binary64_to_double (uint64_t x)
		1524	{
		1525	double r;
		1526
		1527	#if ECB_STDFP
		1528	memcpy (&r, &x, 8);
		1529	#else
		1530	/* emulation, only works for normals and subnormals and +0 */
		1531	int neg = x >> 63;
		1532	int e = (x >> 52) & 0x7ffU;
		1533
		1534	x &= 0xfffffffffffffU;
		1535
		1536	if (e)
		1537	x |= 0x10000000000000U;
		1538	else
		1539	e = 1;
		1540
		1541	/* we distrust ldexp a bit and do the 2**-53 scaling by an extra multiply */
		1542	r = ldexp (x * (0.5 / 0x10000000000000U), e - 1022);
		1543
		1544	r = neg ? -r : r;
		1545	#endif
		1546
		1547	return r;
		1548	}
		1549
		1550	/* convert a float to ieee half/binary16 */
		1551	ecb_function_ ecb_const uint16_t ecb_float_to_binary16 (float x);
		1552	ecb_function_ ecb_const uint16_t
		1553	ecb_float_to_binary16 (float x)
		1554	{
		1555	return ecb_binary32_to_binary16 (ecb_float_to_binary32 (x));
		1556	}
		1557
		1558	/* convert an ieee half/binary16 to float */
		1559	ecb_function_ ecb_const float ecb_binary16_to_float (uint16_t x);
		1560	ecb_function_ ecb_const float
		1561	ecb_binary16_to_float (uint16_t x)
		1562	{
		1563	return ecb_binary32_to_float (ecb_binary16_to_binary32 (x));
		1564	}
		1565
		1566	#endif
		1567
936	#endif	1568	#endif
937		1569
938	/* ECB.H END */	1570	/* ECB.H END */
939		1571
940	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS	1572	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS
941	/* if your architecture doesn't need memory fences, e.g. because it is	1573	/* if your architecture doesn't need memory fences, e.g. because it is
942	* single-cpu/core, or if you use libev in a project that doesn't use libev	1574	* single-cpu/core, or if you use libev in a project that doesn't use libev
943	* from multiple threads, then you can define ECB_AVOID_PTHREADS when compiling	1575	* from multiple threads, then you can define ECB_NO_THREADS when compiling
944	* libev, in which cases the memory fences become nops.	1576	* libev, in which cases the memory fences become nops.
945	* alternatively, you can remove this #error and link against libpthread,	1577	* alternatively, you can remove this #error and link against libpthread,
946	* which will then provide the memory fences.	1578	* which will then provide the memory fences.
947	*/	1579	*/
948	# error "memory fences not defined for your architecture, please report"	1580	# error "memory fences not defined for your architecture, please report"
…		…
952	# define ECB_MEMORY_FENCE do { } while (0)	1584	# define ECB_MEMORY_FENCE do { } while (0)
953	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE	1585	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE
954	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	1586	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
955	#endif	1587	#endif
956		1588
957	#define expect_false(cond) ecb_expect_false (cond)
958	#define expect_true(cond) ecb_expect_true (cond)
959	#define noinline ecb_noinline
960
961	#define inline_size ecb_inline	1589	#define inline_size ecb_inline
962		1590
963	#if EV_FEATURE_CODE	1591	#if EV_FEATURE_CODE
964	# define inline_speed ecb_inline	1592	# define inline_speed ecb_inline
965	#else	1593	#else
966	# define inline_speed static noinline	1594	# define inline_speed ecb_noinline static
967	#endif	1595	#endif
		1596
		1597	/*****************************************************************************/
		1598	/* raw syscall wrappers */
		1599
		1600	#if EV_NEED_SYSCALL
		1601
		1602	#include <sys/syscall.h>
		1603
		1604	/*
		1605	* define some syscall wrappers for common architectures
		1606	* this is mostly for nice looks during debugging, not performance.
		1607	* our syscalls return < 0, not == -1, on error. which is good
		1608	* enough for linux aio.
		1609	* TODO: arm is also common nowadays, maybe even mips and x86
		1610	* TODO: after implementing this, it suddenly looks like overkill, but its hard to remove...
		1611	*/
		1612	#if __GNUC__ && __linux && ECB_AMD64 && !defined __OPTIMIZE_SIZE__
		1613	/* the costly errno access probably kills this for size optimisation */
		1614
		1615	#define ev_syscall(nr,narg,arg1,arg2,arg3,arg4,arg5,arg6) \
		1616	({ \
		1617	long res; \
		1618	register unsigned long r6 __asm__ ("r9" ); \
		1619	register unsigned long r5 __asm__ ("r8" ); \
		1620	register unsigned long r4 __asm__ ("r10"); \
		1621	register unsigned long r3 __asm__ ("rdx"); \
		1622	register unsigned long r2 __asm__ ("rsi"); \
		1623	register unsigned long r1 __asm__ ("rdi"); \
		1624	if (narg >= 6) r6 = (unsigned long)(arg6); \
		1625	if (narg >= 5) r5 = (unsigned long)(arg5); \
		1626	if (narg >= 4) r4 = (unsigned long)(arg4); \
		1627	if (narg >= 3) r3 = (unsigned long)(arg3); \
		1628	if (narg >= 2) r2 = (unsigned long)(arg2); \
		1629	if (narg >= 1) r1 = (unsigned long)(arg1); \
		1630	__asm__ __volatile__ ( \
		1631	"syscall\n\t" \
		1632	: "=a" (res) \
		1633	: "0" (nr), "r" (r1), "r" (r2), "r" (r3), "r" (r4), "r" (r5) \
		1634	: "cc", "r11", "cx", "memory"); \
		1635	errno = -res; \
		1636	res; \
		1637	})
		1638
		1639	#endif
		1640
		1641	#ifdef ev_syscall
		1642	#define ev_syscall0(nr) ev_syscall (nr, 0, 0, 0, 0, 0, 0, 0)
		1643	#define ev_syscall1(nr,arg1) ev_syscall (nr, 1, arg1, 0, 0, 0, 0, 0)
		1644	#define ev_syscall2(nr,arg1,arg2) ev_syscall (nr, 2, arg1, arg2, 0, 0, 0, 0)
		1645	#define ev_syscall3(nr,arg1,arg2,arg3) ev_syscall (nr, 3, arg1, arg2, arg3, 0, 0, 0)
		1646	#define ev_syscall4(nr,arg1,arg2,arg3,arg4) ev_syscall (nr, 3, arg1, arg2, arg3, arg4, 0, 0)
		1647	#define ev_syscall5(nr,arg1,arg2,arg3,arg4,arg5) ev_syscall (nr, 5, arg1, arg2, arg3, arg4, arg5, 0)
		1648	#define ev_syscall6(nr,arg1,arg2,arg3,arg4,arg5,arg6) ev_syscall (nr, 6, arg1, arg2, arg3, arg4, arg5,arg6)
		1649	#else
		1650	#define ev_syscall0(nr) syscall (nr)
		1651	#define ev_syscall1(nr,arg1) syscall (nr, arg1)
		1652	#define ev_syscall2(nr,arg1,arg2) syscall (nr, arg1, arg2)
		1653	#define ev_syscall3(nr,arg1,arg2,arg3) syscall (nr, arg1, arg2, arg3)
		1654	#define ev_syscall4(nr,arg1,arg2,arg3,arg4) syscall (nr, arg1, arg2, arg3, arg4)
		1655	#define ev_syscall5(nr,arg1,arg2,arg3,arg4,arg5) syscall (nr, arg1, arg2, arg3, arg4, arg5)
		1656	#define ev_syscall6(nr,arg1,arg2,arg3,arg4,arg5,arg6) syscall (nr, arg1, arg2, arg3, arg4, arg5,arg6)
		1657	#endif
		1658
		1659	#endif
		1660
		1661	/*****************************************************************************/
968		1662
969	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)	1663	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)
970		1664
971	#if EV_MINPRI == EV_MAXPRI	1665	#if EV_MINPRI == EV_MAXPRI
972	# define ABSPRI(w) (((W)w), 0)	1666	# define ABSPRI(w) (((W)w), 0)
973	#else	1667	#else
974	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)	1668	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)
975	#endif	1669	#endif
976		1670
977	#define EMPTY /* required for microsofts broken pseudo-c compiler */	1671	#define EMPTY /* required for microsofts broken pseudo-c compiler */
978	#define EMPTY2(a,b) /* used to suppress some warnings */
979		1672
980	typedef ev_watcher *W;	1673	typedef ev_watcher *W;
981	typedef ev_watcher_list *WL;	1674	typedef ev_watcher_list *WL;
982	typedef ev_watcher_time *WT;	1675	typedef ev_watcher_time *WT;
983		1676
…		…
1008	# include "ev_win32.c"	1701	# include "ev_win32.c"
1009	#endif	1702	#endif
1010		1703
1011	/*****************************************************************************/	1704	/*****************************************************************************/
1012		1705
		1706	#if EV_USE_LINUXAIO
		1707	# include <linux/aio_abi.h> /* probably only needed for aio_context_t */
		1708	#endif
		1709
1013	/* define a suitable floor function (only used by periodics atm) */	1710	/* define a suitable floor function (only used by periodics atm) */
1014		1711
1015	#if EV_USE_FLOOR	1712	#if EV_USE_FLOOR
1016	# include <math.h>	1713	# include <math.h>
1017	# define ev_floor(v) floor (v)	1714	# define ev_floor(v) floor (v)
1018	#else	1715	#else
1019		1716
1020	#include <float.h>	1717	#include <float.h>
1021		1718
1022	/* a floor() replacement function, should be independent of ev_tstamp type */	1719	/* a floor() replacement function, should be independent of ev_tstamp type */
		1720	ecb_noinline
1023	static ev_tstamp noinline	1721	static ev_tstamp
1024	ev_floor (ev_tstamp v)	1722	ev_floor (ev_tstamp v)
1025	{	1723	{
1026	/* the choice of shift factor is not terribly important */	1724	/* the choice of shift factor is not terribly important */
1027	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */	1725	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */
1028	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;	1726	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;
1029	#else	1727	#else
1030	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;	1728	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;
1031	#endif	1729	#endif
1032		1730
		1731	/* special treatment for negative arguments */
		1732	if (ecb_expect_false (v < 0.))
		1733	{
		1734	ev_tstamp f = -ev_floor (-v);
		1735
		1736	return f - (f == v ? 0 : 1);
		1737	}
		1738
1033	/* argument too large for an unsigned long? */	1739	/* argument too large for an unsigned long? then reduce it */
1034	if (expect_false (v >= shift))	1740	if (ecb_expect_false (v >= shift))
1035	{	1741	{
1036	ev_tstamp f;	1742	ev_tstamp f;
1037		1743
1038	if (v == v - 1.)	1744	if (v == v - 1.)
1039	return v; /* very large number */	1745	return v; /* very large numbers are assumed to be integer */
1040		1746
1041	f = shift * ev_floor (v * (1. / shift));	1747	f = shift * ev_floor (v * (1. / shift));
1042	return f + ev_floor (v - f);	1748	return f + ev_floor (v - f);
1043	}	1749	}
1044		1750
1045	/* special treatment for negative args? */
1046	if (expect_false (v < 0.))
1047	{
1048	ev_tstamp f = -ev_floor (-v);
1049
1050	return f - (f == v ? 0 : 1);
1051	}
1052
1053	/* fits into an unsigned long */	1751	/* fits into an unsigned long */
1054	return (unsigned long)v;	1752	return (unsigned long)v;
1055	}	1753	}
1056		1754
1057	#endif	1755	#endif
…		…
1060		1758
1061	#ifdef __linux	1759	#ifdef __linux
1062	# include <sys/utsname.h>	1760	# include <sys/utsname.h>
1063	#endif	1761	#endif
1064		1762
1065	static unsigned int noinline ecb_cold	1763	ecb_noinline ecb_cold
		1764	static unsigned int
1066	ev_linux_version (void)	1765	ev_linux_version (void)
1067	{	1766	{
1068	#ifdef __linux	1767	#ifdef __linux
1069	unsigned int v = 0;	1768	unsigned int v = 0;
1070	struct utsname buf;	1769	struct utsname buf;
…		…
1099	}	1798	}
1100		1799
1101	/*****************************************************************************/	1800	/*****************************************************************************/
1102		1801
1103	#if EV_AVOID_STDIO	1802	#if EV_AVOID_STDIO
1104	static void noinline ecb_cold	1803	ecb_noinline ecb_cold
		1804	static void
1105	ev_printerr (const char *msg)	1805	ev_printerr (const char *msg)
1106	{	1806	{
1107	write (STDERR_FILENO, msg, strlen (msg));	1807	write (STDERR_FILENO, msg, strlen (msg));
1108	}	1808	}
1109	#endif	1809	#endif
1110		1810
1111	static void (*syserr_cb)(const char *msg) EV_THROW;	1811	static void (*syserr_cb)(const char *msg) EV_NOEXCEPT;
1112		1812
1113	void ecb_cold	1813	ecb_cold
		1814	void
1114	ev_set_syserr_cb (void (*cb)(const char *msg)) EV_THROW	1815	ev_set_syserr_cb (void (*cb)(const char *msg) EV_NOEXCEPT) EV_NOEXCEPT
1115	{	1816	{
1116	syserr_cb = cb;	1817	syserr_cb = cb;
1117	}	1818	}
1118		1819
1119	static void noinline ecb_cold	1820	ecb_noinline ecb_cold
		1821	static void
1120	ev_syserr (const char *msg)	1822	ev_syserr (const char *msg)
1121	{	1823	{
1122	if (!msg)	1824	if (!msg)
1123	msg = "(libev) system error";	1825	msg = "(libev) system error";
1124		1826
…		…
1137	abort ();	1839	abort ();
1138	}	1840	}
1139	}	1841	}
1140		1842
1141	static void *	1843	static void *
1142	ev_realloc_emul (void *ptr, long size)	1844	ev_realloc_emul (void *ptr, long size) EV_NOEXCEPT
1143	{	1845	{
1144	#if __GLIBC__
1145	return realloc (ptr, size);
1146	#else
1147	/* some systems, notably openbsd and darwin, fail to properly	1846	/* some systems, notably openbsd and darwin, fail to properly
1148	* implement realloc (x, 0) (as required by both ansi c-89 and	1847	* implement realloc (x, 0) (as required by both ansi c-89 and
1149	* the single unix specification, so work around them here.	1848	* the single unix specification, so work around them here.
		1849	* recently, also (at least) fedora and debian started breaking it,
		1850	* despite documenting it otherwise.
1150	*/	1851	*/
1151		1852
1152	if (size)	1853	if (size)
1153	return realloc (ptr, size);	1854	return realloc (ptr, size);
1154		1855
1155	free (ptr);	1856	free (ptr);
1156	return 0;	1857	return 0;
1157	#endif
1158	}	1858	}
1159		1859
1160	static void *(*alloc)(void *ptr, long size) EV_THROW = ev_realloc_emul;	1860	static void *(*alloc)(void *ptr, long size) EV_NOEXCEPT = ev_realloc_emul;
1161		1861
1162	void ecb_cold	1862	ecb_cold
		1863	void
1163	ev_set_allocator (void *(*cb)(void *ptr, long size)) EV_THROW	1864	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_NOEXCEPT) EV_NOEXCEPT
1164	{	1865	{
1165	alloc = cb;	1866	alloc = cb;
1166	}	1867	}
1167		1868
1168	inline_speed void *	1869	inline_speed void *
…		…
1195	typedef struct	1896	typedef struct
1196	{	1897	{
1197	WL head;	1898	WL head;
1198	unsigned char events; /* the events watched for */	1899	unsigned char events; /* the events watched for */
1199	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */	1900	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */
1200	unsigned char emask; /* the epoll backend stores the actual kernel mask in here */	1901	unsigned char emask; /* some backends store the actual kernel mask in here */
1201	unsigned char unused;	1902	unsigned char eflags; /* flags field for use by backends */
1202	#if EV_USE_EPOLL	1903	#if EV_USE_EPOLL
1203	unsigned int egen; /* generation counter to counter epoll bugs */	1904	unsigned int egen; /* generation counter to counter epoll bugs */
1204	#endif	1905	#endif
1205	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP	1906	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP
1206	SOCKET handle;	1907	SOCKET handle;
…		…
1270	static int ev_default_loop_ptr;	1971	static int ev_default_loop_ptr;
1271		1972
1272	#endif	1973	#endif
1273		1974
1274	#if EV_FEATURE_API	1975	#if EV_FEATURE_API
1275	# define EV_RELEASE_CB if (expect_false (release_cb)) release_cb (EV_A)	1976	# define EV_RELEASE_CB if (ecb_expect_false (release_cb)) release_cb (EV_A)
1276	# define EV_ACQUIRE_CB if (expect_false (acquire_cb)) acquire_cb (EV_A)	1977	# define EV_ACQUIRE_CB if (ecb_expect_false (acquire_cb)) acquire_cb (EV_A)
1277	# define EV_INVOKE_PENDING invoke_cb (EV_A)	1978	# define EV_INVOKE_PENDING invoke_cb (EV_A)
1278	#else	1979	#else
1279	# define EV_RELEASE_CB (void)0	1980	# define EV_RELEASE_CB (void)0
1280	# define EV_ACQUIRE_CB (void)0	1981	# define EV_ACQUIRE_CB (void)0
1281	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)	1982	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)
…		…
1285		1986
1286	/*****************************************************************************/	1987	/*****************************************************************************/
1287		1988
1288	#ifndef EV_HAVE_EV_TIME	1989	#ifndef EV_HAVE_EV_TIME
1289	ev_tstamp	1990	ev_tstamp
1290	ev_time (void) EV_THROW	1991	ev_time (void) EV_NOEXCEPT
1291	{	1992	{
1292	#if EV_USE_REALTIME	1993	#if EV_USE_REALTIME
1293	if (expect_true (have_realtime))	1994	if (ecb_expect_true (have_realtime))
1294	{	1995	{
1295	struct timespec ts;	1996	struct timespec ts;
1296	clock_gettime (CLOCK_REALTIME, &ts);	1997	clock_gettime (CLOCK_REALTIME, &ts);
1297	return ts.tv_sec + ts.tv_nsec * 1e-9;	1998	return ts.tv_sec + ts.tv_nsec * 1e-9;
1298	}	1999	}
…		…
1306		2007
1307	inline_size ev_tstamp	2008	inline_size ev_tstamp
1308	get_clock (void)	2009	get_clock (void)
1309	{	2010	{
1310	#if EV_USE_MONOTONIC	2011	#if EV_USE_MONOTONIC
1311	if (expect_true (have_monotonic))	2012	if (ecb_expect_true (have_monotonic))
1312	{	2013	{
1313	struct timespec ts;	2014	struct timespec ts;
1314	clock_gettime (CLOCK_MONOTONIC, &ts);	2015	clock_gettime (CLOCK_MONOTONIC, &ts);
1315	return ts.tv_sec + ts.tv_nsec * 1e-9;	2016	return ts.tv_sec + ts.tv_nsec * 1e-9;
1316	}	2017	}
…		…
1319	return ev_time ();	2020	return ev_time ();
1320	}	2021	}
1321		2022
1322	#if EV_MULTIPLICITY	2023	#if EV_MULTIPLICITY
1323	ev_tstamp	2024	ev_tstamp
1324	ev_now (EV_P) EV_THROW	2025	ev_now (EV_P) EV_NOEXCEPT
1325	{	2026	{
1326	return ev_rt_now;	2027	return ev_rt_now;
1327	}	2028	}
1328	#endif	2029	#endif
1329		2030
1330	void	2031	void
1331	ev_sleep (ev_tstamp delay) EV_THROW	2032	ev_sleep (ev_tstamp delay) EV_NOEXCEPT
1332	{	2033	{
1333	if (delay > 0.)	2034	if (delay > 0.)
1334	{	2035	{
1335	#if EV_USE_NANOSLEEP	2036	#if EV_USE_NANOSLEEP
1336	struct timespec ts;	2037	struct timespec ts;
1337		2038
1338	EV_TS_SET (ts, delay);	2039	EV_TS_SET (ts, delay);
1339	nanosleep (&ts, 0);	2040	nanosleep (&ts, 0);
1340	#elif defined _WIN32	2041	#elif defined _WIN32
		2042	/* maybe this should round up, as ms is very low resolution */
		2043	/* compared to select (µs) or nanosleep (ns) */
1341	Sleep ((unsigned long)(delay * 1e3));	2044	Sleep ((unsigned long)(delay * 1e3));
1342	#else	2045	#else
1343	struct timeval tv;	2046	struct timeval tv;
1344		2047
1345	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */	2048	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */
…		…
1376	}	2079	}
1377		2080
1378	return ncur;	2081	return ncur;
1379	}	2082	}
1380		2083
1381	static void * noinline ecb_cold	2084	ecb_noinline ecb_cold
		2085	static void *
1382	array_realloc (int elem, void *base, int *cur, int cnt)	2086	array_realloc (int elem, void *base, int *cur, int cnt)
1383	{	2087	{
1384	*cur = array_nextsize (elem, *cur, cnt);	2088	*cur = array_nextsize (elem, *cur, cnt);
1385	return ev_realloc (base, elem * *cur);	2089	return ev_realloc (base, elem * *cur);
1386	}	2090	}
1387		2091
		2092	#define array_needsize_noinit(base,offset,count)
		2093
1388	#define array_init_zero(base,count) \	2094	#define array_needsize_zerofill(base,offset,count) \
1389	memset ((void *)(base), 0, sizeof (*(base)) * (count))	2095	memset ((void *)(base + offset), 0, sizeof (*(base)) * (count))
1390		2096
1391	#define array_needsize(type,base,cur,cnt,init) \	2097	#define array_needsize(type,base,cur,cnt,init) \
1392	if (expect_false ((cnt) > (cur))) \	2098	if (ecb_expect_false ((cnt) > (cur))) \
1393	{ \	2099	{ \
1394	int ecb_unused ocur_ = (cur); \	2100	ecb_unused int ocur_ = (cur); \
1395	(base) = (type *)array_realloc \	2101	(base) = (type *)array_realloc \
1396	(sizeof (type), (base), &(cur), (cnt)); \	2102	(sizeof (type), (base), &(cur), (cnt)); \
1397	init ((base) + (ocur_), (cur) - ocur_); \	2103	init ((base), ocur_, ((cur) - ocur_)); \
1398	}	2104	}
1399		2105
1400	#if 0	2106	#if 0
1401	#define array_slim(type,stem) \	2107	#define array_slim(type,stem) \
1402	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \	2108	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \
…		…
1411	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0	2117	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0
1412		2118
1413	/*****************************************************************************/	2119	/*****************************************************************************/
1414		2120
1415	/* dummy callback for pending events */	2121	/* dummy callback for pending events */
1416	static void noinline	2122	ecb_noinline
		2123	static void
1417	pendingcb (EV_P_ ev_prepare *w, int revents)	2124	pendingcb (EV_P_ ev_prepare *w, int revents)
1418	{	2125	{
1419	}	2126	}
1420		2127
1421	void noinline	2128	ecb_noinline
		2129	void
1422	ev_feed_event (EV_P_ void *w, int revents) EV_THROW	2130	ev_feed_event (EV_P_ void *w, int revents) EV_NOEXCEPT
1423	{	2131	{
1424	W w_ = (W)w;	2132	W w_ = (W)w;
1425	int pri = ABSPRI (w_);	2133	int pri = ABSPRI (w_);
1426		2134
1427	if (expect_false (w_->pending))	2135	if (ecb_expect_false (w_->pending))
1428	pendings [pri][w_->pending - 1].events |= revents;	2136	pendings [pri][w_->pending - 1].events |= revents;
1429	else	2137	else
1430	{	2138	{
1431	w_->pending = ++pendingcnt [pri];	2139	w_->pending = ++pendingcnt [pri];
1432	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, EMPTY2);	2140	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, array_needsize_noinit);
1433	pendings [pri][w_->pending - 1].w = w_;	2141	pendings [pri][w_->pending - 1].w = w_;
1434	pendings [pri][w_->pending - 1].events = revents;	2142	pendings [pri][w_->pending - 1].events = revents;
1435	}	2143	}
1436		2144
1437	pendingpri = NUMPRI - 1;	2145	pendingpri = NUMPRI - 1;
1438	}	2146	}
1439		2147
1440	inline_speed void	2148	inline_speed void
1441	feed_reverse (EV_P_ W w)	2149	feed_reverse (EV_P_ W w)
1442	{	2150	{
1443	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, EMPTY2);	2151	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, array_needsize_noinit);
1444	rfeeds [rfeedcnt++] = w;	2152	rfeeds [rfeedcnt++] = w;
1445	}	2153	}
1446		2154
1447	inline_size void	2155	inline_size void
1448	feed_reverse_done (EV_P_ int revents)	2156	feed_reverse_done (EV_P_ int revents)
…		…
1483	inline_speed void	2191	inline_speed void
1484	fd_event (EV_P_ int fd, int revents)	2192	fd_event (EV_P_ int fd, int revents)
1485	{	2193	{
1486	ANFD *anfd = anfds + fd;	2194	ANFD *anfd = anfds + fd;
1487		2195
1488	if (expect_true (!anfd->reify))	2196	if (ecb_expect_true (!anfd->reify))
1489	fd_event_nocheck (EV_A_ fd, revents);	2197	fd_event_nocheck (EV_A_ fd, revents);
1490	}	2198	}
1491		2199
1492	void	2200	void
1493	ev_feed_fd_event (EV_P_ int fd, int revents) EV_THROW	2201	ev_feed_fd_event (EV_P_ int fd, int revents) EV_NOEXCEPT
1494	{	2202	{
1495	if (fd >= 0 && fd < anfdmax)	2203	if (fd >= 0 && fd < anfdmax)
1496	fd_event_nocheck (EV_A_ fd, revents);	2204	fd_event_nocheck (EV_A_ fd, revents);
1497	}	2205	}
1498		2206
…		…
1535	ev_io *w;	2243	ev_io *w;
1536		2244
1537	unsigned char o_events = anfd->events;	2245	unsigned char o_events = anfd->events;
1538	unsigned char o_reify = anfd->reify;	2246	unsigned char o_reify = anfd->reify;
1539		2247
1540	anfd->reify = 0;	2248	anfd->reify = 0;
1541		2249
1542	/*if (expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */	2250	/*if (ecb_expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */
1543	{	2251	{
1544	anfd->events = 0;	2252	anfd->events = 0;
1545		2253
1546	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)	2254	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)
1547	anfd->events |= (unsigned char)w->events;	2255	anfd->events |= (unsigned char)w->events;
…		…
1556		2264
1557	fdchangecnt = 0;	2265	fdchangecnt = 0;
1558	}	2266	}
1559		2267
1560	/* something about the given fd changed */	2268	/* something about the given fd changed */
1561	inline_size void	2269	inline_size
		2270	void
1562	fd_change (EV_P_ int fd, int flags)	2271	fd_change (EV_P_ int fd, int flags)
1563	{	2272	{
1564	unsigned char reify = anfds [fd].reify;	2273	unsigned char reify = anfds [fd].reify;
1565	anfds [fd].reify |= flags;	2274	anfds [fd].reify |= flags;
1566		2275
1567	if (expect_true (!reify))	2276	if (ecb_expect_true (!reify))
1568	{	2277	{
1569	++fdchangecnt;	2278	++fdchangecnt;
1570	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, EMPTY2);	2279	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, array_needsize_noinit);
1571	fdchanges [fdchangecnt - 1] = fd;	2280	fdchanges [fdchangecnt - 1] = fd;
1572	}	2281	}
1573	}	2282	}
1574		2283
1575	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */	2284	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */
1576	inline_speed void ecb_cold	2285	inline_speed ecb_cold void
1577	fd_kill (EV_P_ int fd)	2286	fd_kill (EV_P_ int fd)
1578	{	2287	{
1579	ev_io *w;	2288	ev_io *w;
1580		2289
1581	while ((w = (ev_io *)anfds [fd].head))	2290	while ((w = (ev_io *)anfds [fd].head))
…		…
1584	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);	2293	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);
1585	}	2294	}
1586	}	2295	}
1587		2296
1588	/* check whether the given fd is actually valid, for error recovery */	2297	/* check whether the given fd is actually valid, for error recovery */
1589	inline_size int ecb_cold	2298	inline_size ecb_cold int
1590	fd_valid (int fd)	2299	fd_valid (int fd)
1591	{	2300	{
1592	#ifdef _WIN32	2301	#ifdef _WIN32
1593	return EV_FD_TO_WIN32_HANDLE (fd) != -1;	2302	return EV_FD_TO_WIN32_HANDLE (fd) != -1;
1594	#else	2303	#else
1595	return fcntl (fd, F_GETFD) != -1;	2304	return fcntl (fd, F_GETFD) != -1;
1596	#endif	2305	#endif
1597	}	2306	}
1598		2307
1599	/* called on EBADF to verify fds */	2308	/* called on EBADF to verify fds */
1600	static void noinline ecb_cold	2309	ecb_noinline ecb_cold
		2310	static void
1601	fd_ebadf (EV_P)	2311	fd_ebadf (EV_P)
1602	{	2312	{
1603	int fd;	2313	int fd;
1604		2314
1605	for (fd = 0; fd < anfdmax; ++fd)	2315	for (fd = 0; fd < anfdmax; ++fd)
…		…
1607	if (!fd_valid (fd) && errno == EBADF)	2317	if (!fd_valid (fd) && errno == EBADF)
1608	fd_kill (EV_A_ fd);	2318	fd_kill (EV_A_ fd);
1609	}	2319	}
1610		2320
1611	/* called on ENOMEM in select/poll to kill some fds and retry */	2321	/* called on ENOMEM in select/poll to kill some fds and retry */
1612	static void noinline ecb_cold	2322	ecb_noinline ecb_cold
		2323	static void
1613	fd_enomem (EV_P)	2324	fd_enomem (EV_P)
1614	{	2325	{
1615	int fd;	2326	int fd;
1616		2327
1617	for (fd = anfdmax; fd--; )	2328	for (fd = anfdmax; fd--; )
…		…
1621	break;	2332	break;
1622	}	2333	}
1623	}	2334	}
1624		2335
1625	/* usually called after fork if backend needs to re-arm all fds from scratch */	2336	/* usually called after fork if backend needs to re-arm all fds from scratch */
1626	static void noinline	2337	ecb_noinline
		2338	static void
1627	fd_rearm_all (EV_P)	2339	fd_rearm_all (EV_P)
1628	{	2340	{
1629	int fd;	2341	int fd;
1630		2342
1631	for (fd = 0; fd < anfdmax; ++fd)	2343	for (fd = 0; fd < anfdmax; ++fd)
…		…
1684	ev_tstamp minat;	2396	ev_tstamp minat;
1685	ANHE *minpos;	2397	ANHE *minpos;
1686	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;	2398	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;
1687		2399
1688	/* find minimum child */	2400	/* find minimum child */
1689	if (expect_true (pos + DHEAP - 1 < E))	2401	if (ecb_expect_true (pos + DHEAP - 1 < E))
1690	{	2402	{
1691	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));	2403	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));
1692	if ( ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));	2404	if ( ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));
1693	if ( ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));	2405	if ( ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));
1694	if ( ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));	2406	if ( ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));
…		…
1812		2524
1813	/*****************************************************************************/	2525	/*****************************************************************************/
1814		2526
1815	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	2527	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
1816		2528
1817	static void noinline ecb_cold	2529	ecb_noinline ecb_cold
		2530	static void
1818	evpipe_init (EV_P)	2531	evpipe_init (EV_P)
1819	{	2532	{
1820	if (!ev_is_active (&pipe_w))	2533	if (!ev_is_active (&pipe_w))
1821	{	2534	{
		2535	int fds [2];
		2536
1822	# if EV_USE_EVENTFD	2537	# if EV_USE_EVENTFD
		2538	fds [0] = -1;
1823	evfd = eventfd (0, EFD_NONBLOCK | EFD_CLOEXEC);	2539	fds [1] = eventfd (0, EFD_NONBLOCK | EFD_CLOEXEC);
1824	if (evfd < 0 && errno == EINVAL)	2540	if (fds [1] < 0 && errno == EINVAL)
1825	evfd = eventfd (0, 0);	2541	fds [1] = eventfd (0, 0);
1826		2542
1827	if (evfd >= 0)	2543	if (fds [1] < 0)
1828	{
1829	evpipe [0] = -1;
1830	fd_intern (evfd); /* doing it twice doesn't hurt */
1831	ev_io_set (&pipe_w, evfd, EV_READ);
1832	}
1833	else
1834	# endif	2544	# endif
1835	{	2545	{
1836	while (pipe (evpipe))	2546	while (pipe (fds))
1837	ev_syserr ("(libev) error creating signal/async pipe");	2547	ev_syserr ("(libev) error creating signal/async pipe");
1838		2548
1839	fd_intern (evpipe [0]);	2549	fd_intern (fds [0]);
1840	fd_intern (evpipe [1]);
1841	ev_io_set (&pipe_w, evpipe [0], EV_READ);
1842	}	2550	}
1843		2551
		2552	evpipe [0] = fds [0];
		2553
		2554	if (evpipe [1] < 0)
		2555	evpipe [1] = fds [1]; /* first call, set write fd */
		2556	else
		2557	{
		2558	/* on subsequent calls, do not change evpipe [1] */
		2559	/* so that evpipe_write can always rely on its value. */
		2560	/* this branch does not do anything sensible on windows, */
		2561	/* so must not be executed on windows */
		2562
		2563	dup2 (fds [1], evpipe [1]);
		2564	close (fds [1]);
		2565	}
		2566
		2567	fd_intern (evpipe [1]);
		2568
		2569	ev_io_set (&pipe_w, evpipe [0] < 0 ? evpipe [1] : evpipe [0], EV_READ);
1844	ev_io_start (EV_A_ &pipe_w);	2570	ev_io_start (EV_A_ &pipe_w);
1845	ev_unref (EV_A); /* watcher should not keep loop alive */	2571	ev_unref (EV_A); /* watcher should not keep loop alive */
1846	}	2572	}
1847	}	2573	}
1848		2574
1849	inline_speed void	2575	inline_speed void
1850	evpipe_write (EV_P_ EV_ATOMIC_T *flag)	2576	evpipe_write (EV_P_ EV_ATOMIC_T *flag)
1851	{	2577	{
1852	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */	2578	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */
1853		2579
1854	if (expect_true (*flag))	2580	if (ecb_expect_true (*flag))
1855	return;	2581	return;
1856		2582
1857	*flag = 1;	2583	*flag = 1;
1858
1859	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */	2584	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */
1860		2585
1861	pipe_write_skipped = 1;	2586	pipe_write_skipped = 1;
1862		2587
1863	ECB_MEMORY_FENCE; /* make sure pipe_write_skipped is visible before we check pipe_write_wanted */	2588	ECB_MEMORY_FENCE; /* make sure pipe_write_skipped is visible before we check pipe_write_wanted */
1864		2589
1865	if (pipe_write_wanted)	2590	if (pipe_write_wanted)
1866	{	2591	{
1867	int old_errno;	2592	int old_errno;
1868		2593
1869	pipe_write_skipped = 0; /* just an optimisation, no fence needed */	2594	pipe_write_skipped = 0;
		2595	ECB_MEMORY_FENCE_RELEASE;
1870		2596
1871	old_errno = errno; /* save errno because write will clobber it */	2597	old_errno = errno; /* save errno because write will clobber it */
1872		2598
1873	#if EV_USE_EVENTFD	2599	#if EV_USE_EVENTFD
1874	if (evfd >= 0)	2600	if (evpipe [0] < 0)
1875	{	2601	{
1876	uint64_t counter = 1;	2602	uint64_t counter = 1;
1877	write (evfd, &counter, sizeof (uint64_t));	2603	write (evpipe [1], &counter, sizeof (uint64_t));
1878	}	2604	}
1879	else	2605	else
1880	#endif	2606	#endif
1881	{	2607	{
1882	#ifdef _WIN32	2608	#ifdef _WIN32
1883	WSABUF buf;	2609	WSABUF buf;
1884	DWORD sent;	2610	DWORD sent;
1885	buf.buf = &buf;	2611	buf.buf = (char *)&buf;
1886	buf.len = 1;	2612	buf.len = 1;
1887	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);	2613	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);
1888	#else	2614	#else
1889	write (evpipe [1], &(evpipe [1]), 1);	2615	write (evpipe [1], &(evpipe [1]), 1);
1890	#endif	2616	#endif
…		…
1902	int i;	2628	int i;
1903		2629
1904	if (revents & EV_READ)	2630	if (revents & EV_READ)
1905	{	2631	{
1906	#if EV_USE_EVENTFD	2632	#if EV_USE_EVENTFD
1907	if (evfd >= 0)	2633	if (evpipe [0] < 0)
1908	{	2634	{
1909	uint64_t counter;	2635	uint64_t counter;
1910	read (evfd, &counter, sizeof (uint64_t));	2636	read (evpipe [1], &counter, sizeof (uint64_t));
1911	}	2637	}
1912	else	2638	else
1913	#endif	2639	#endif
1914	{	2640	{
1915	char dummy[4];	2641	char dummy[4];
1916	#ifdef _WIN32	2642	#ifdef _WIN32
1917	WSABUF buf;	2643	WSABUF buf;
1918	DWORD recvd;	2644	DWORD recvd;
		2645	DWORD flags = 0;
1919	buf.buf = dummy;	2646	buf.buf = dummy;
1920	buf.len = sizeof (dummy);	2647	buf.len = sizeof (dummy);
1921	WSARecv (EV_FD_TO_WIN32_HANDLE (evpipe [0]), &buf, 1, &recvd, 0, 0, 0);	2648	WSARecv (EV_FD_TO_WIN32_HANDLE (evpipe [0]), &buf, 1, &recvd, &flags, 0, 0);
1922	#else	2649	#else
1923	read (evpipe [0], &dummy, sizeof (dummy));	2650	read (evpipe [0], &dummy, sizeof (dummy));
1924	#endif	2651	#endif
1925	}	2652	}
1926	}	2653	}
…		…
1932	#if EV_SIGNAL_ENABLE	2659	#if EV_SIGNAL_ENABLE
1933	if (sig_pending)	2660	if (sig_pending)
1934	{	2661	{
1935	sig_pending = 0;	2662	sig_pending = 0;
1936		2663
1937	ECB_MEMORY_FENCE_RELEASE;	2664	ECB_MEMORY_FENCE;
1938		2665
1939	for (i = EV_NSIG - 1; i--; )	2666	for (i = EV_NSIG - 1; i--; )
1940	if (expect_false (signals [i].pending))	2667	if (ecb_expect_false (signals [i].pending))
1941	ev_feed_signal_event (EV_A_ i + 1);	2668	ev_feed_signal_event (EV_A_ i + 1);
1942	}	2669	}
1943	#endif	2670	#endif
1944		2671
1945	#if EV_ASYNC_ENABLE	2672	#if EV_ASYNC_ENABLE
1946	if (async_pending)	2673	if (async_pending)
1947	{	2674	{
1948	async_pending = 0;	2675	async_pending = 0;
1949		2676
1950	ECB_MEMORY_FENCE_RELEASE;	2677	ECB_MEMORY_FENCE;
1951		2678
1952	for (i = asynccnt; i--; )	2679	for (i = asynccnt; i--; )
1953	if (asyncs [i]->sent)	2680	if (asyncs [i]->sent)
1954	{	2681	{
1955	asyncs [i]->sent = 0;	2682	asyncs [i]->sent = 0;
		2683	ECB_MEMORY_FENCE_RELEASE;
1956	ev_feed_event (EV_A_ asyncs [i], EV_ASYNC);	2684	ev_feed_event (EV_A_ asyncs [i], EV_ASYNC);
1957	}	2685	}
1958	}	2686	}
1959	#endif	2687	#endif
1960	}	2688	}
1961		2689
1962	/*****************************************************************************/	2690	/*****************************************************************************/
1963		2691
1964	void	2692	void
1965	ev_feed_signal (int signum) EV_THROW	2693	ev_feed_signal (int signum) EV_NOEXCEPT
1966	{	2694	{
1967	#if EV_MULTIPLICITY	2695	#if EV_MULTIPLICITY
		2696	EV_P;
		2697	ECB_MEMORY_FENCE_ACQUIRE;
1968	EV_P = signals [signum - 1].loop;	2698	EV_A = signals [signum - 1].loop;
1969		2699
1970	if (!EV_A)	2700	if (!EV_A)
1971	return;	2701	return;
1972	#endif	2702	#endif
1973		2703
1974	if (!ev_active (&pipe_w))
1975	return;
1976
1977	signals [signum - 1].pending = 1;	2704	signals [signum - 1].pending = 1;
1978	evpipe_write (EV_A_ &sig_pending);	2705	evpipe_write (EV_A_ &sig_pending);
1979	}	2706	}
1980		2707
1981	static void	2708	static void
…		…
1986	#endif	2713	#endif
1987		2714
1988	ev_feed_signal (signum);	2715	ev_feed_signal (signum);
1989	}	2716	}
1990		2717
1991	void noinline	2718	ecb_noinline
		2719	void
1992	ev_feed_signal_event (EV_P_ int signum) EV_THROW	2720	ev_feed_signal_event (EV_P_ int signum) EV_NOEXCEPT
1993	{	2721	{
1994	WL w;	2722	WL w;
1995		2723
1996	if (expect_false (signum <= 0 || signum > EV_NSIG))	2724	if (ecb_expect_false (signum <= 0 || signum >= EV_NSIG))
1997	return;	2725	return;
1998		2726
1999	--signum;	2727	--signum;
2000		2728
2001	#if EV_MULTIPLICITY	2729	#if EV_MULTIPLICITY
2002	/* it is permissible to try to feed a signal to the wrong loop */	2730	/* it is permissible to try to feed a signal to the wrong loop */
2003	/* or, likely more useful, feeding a signal nobody is waiting for */	2731	/* or, likely more useful, feeding a signal nobody is waiting for */
2004		2732
2005	if (expect_false (signals [signum].loop != EV_A))	2733	if (ecb_expect_false (signals [signum].loop != EV_A))
2006	return;	2734	return;
2007	#endif	2735	#endif
2008		2736
2009	signals [signum].pending = 0;	2737	signals [signum].pending = 0;
		2738	ECB_MEMORY_FENCE_RELEASE;
2010		2739
2011	for (w = signals [signum].head; w; w = w->next)	2740	for (w = signals [signum].head; w; w = w->next)
2012	ev_feed_event (EV_A_ (W)w, EV_SIGNAL);	2741	ev_feed_event (EV_A_ (W)w, EV_SIGNAL);
2013	}	2742	}
2014		2743
…		…
2105	# include "ev_kqueue.c"	2834	# include "ev_kqueue.c"
2106	#endif	2835	#endif
2107	#if EV_USE_EPOLL	2836	#if EV_USE_EPOLL
2108	# include "ev_epoll.c"	2837	# include "ev_epoll.c"
2109	#endif	2838	#endif
		2839	#if EV_USE_LINUXAIO
		2840	# include "ev_linuxaio.c"
		2841	#endif
		2842	#if EV_USE_IOURING
		2843	# include "ev_iouring.c"
		2844	#endif
2110	#if EV_USE_POLL	2845	#if EV_USE_POLL
2111	# include "ev_poll.c"	2846	# include "ev_poll.c"
2112	#endif	2847	#endif
2113	#if EV_USE_SELECT	2848	#if EV_USE_SELECT
2114	# include "ev_select.c"	2849	# include "ev_select.c"
2115	#endif	2850	#endif
2116		2851
2117	int ecb_cold	2852	ecb_cold int
2118	ev_version_major (void) EV_THROW	2853	ev_version_major (void) EV_NOEXCEPT
2119	{	2854	{
2120	return EV_VERSION_MAJOR;	2855	return EV_VERSION_MAJOR;
2121	}	2856	}
2122		2857
2123	int ecb_cold	2858	ecb_cold int
2124	ev_version_minor (void) EV_THROW	2859	ev_version_minor (void) EV_NOEXCEPT
2125	{	2860	{
2126	return EV_VERSION_MINOR;	2861	return EV_VERSION_MINOR;
2127	}	2862	}
2128		2863
2129	/* return true if we are running with elevated privileges and should ignore env variables */	2864	/* return true if we are running with elevated privileges and should ignore env variables */
2130	int inline_size ecb_cold	2865	inline_size ecb_cold int
2131	enable_secure (void)	2866	enable_secure (void)
2132	{	2867	{
2133	#ifdef _WIN32	2868	#ifdef _WIN32
2134	return 0;	2869	return 0;
2135	#else	2870	#else
2136	return getuid () != geteuid ()	2871	return getuid () != geteuid ()
2137	|| getgid () != getegid ();	2872	|| getgid () != getegid ();
2138	#endif	2873	#endif
2139	}	2874	}
2140		2875
2141	unsigned int ecb_cold	2876	ecb_cold
		2877	unsigned int
2142	ev_supported_backends (void) EV_THROW	2878	ev_supported_backends (void) EV_NOEXCEPT
2143	{	2879	{
2144	unsigned int flags = 0;	2880	unsigned int flags = 0;
2145		2881
2146	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;	2882	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;
2147	if (EV_USE_KQUEUE) flags |= EVBACKEND_KQUEUE;	2883	if (EV_USE_KQUEUE ) flags |= EVBACKEND_KQUEUE;
2148	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;	2884	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;
		2885	if (EV_USE_LINUXAIO) flags |= EVBACKEND_LINUXAIO;
		2886	if (EV_USE_IOURING ) flags |= EVBACKEND_IOURING;
2149	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;	2887	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;
2150	if (EV_USE_SELECT) flags |= EVBACKEND_SELECT;	2888	if (EV_USE_SELECT ) flags |= EVBACKEND_SELECT;
2151		2889
2152	return flags;	2890	return flags;
2153	}	2891	}
2154		2892
2155	unsigned int ecb_cold	2893	ecb_cold
		2894	unsigned int
2156	ev_recommended_backends (void) EV_THROW	2895	ev_recommended_backends (void) EV_NOEXCEPT
2157	{	2896	{
2158	unsigned int flags = ev_supported_backends ();	2897	unsigned int flags = ev_supported_backends ();
2159		2898
2160	#ifndef __NetBSD__	2899	#ifndef __NetBSD__
2161	/* kqueue is borked on everything but netbsd apparently */	2900	/* kqueue is borked on everything but netbsd apparently */
…		…
2169	#endif	2908	#endif
2170	#ifdef __FreeBSD__	2909	#ifdef __FreeBSD__
2171	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */	2910	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */
2172	#endif	2911	#endif
2173		2912
		2913	/* TODO: linuxaio is very experimental */
		2914	#if !EV_RECOMMEND_LINUXAIO
		2915	flags &= ~EVBACKEND_LINUXAIO;
		2916	#endif
		2917	/* TODO: linuxaio is super experimental */
		2918	#if !EV_RECOMMEND_IOURING
		2919	flags &= ~EVBACKEND_IOURING;
		2920	#endif
		2921
2174	return flags;	2922	return flags;
2175	}	2923	}
2176		2924
2177	unsigned int ecb_cold	2925	ecb_cold
		2926	unsigned int
2178	ev_embeddable_backends (void) EV_THROW	2927	ev_embeddable_backends (void) EV_NOEXCEPT
2179	{	2928	{
2180	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;	2929	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;
2181		2930
2182	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */	2931	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */
2183	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */	2932	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */
2184	flags &= ~EVBACKEND_EPOLL;	2933	flags &= ~EVBACKEND_EPOLL;
2185		2934
		2935	/* EVBACKEND_LINUXAIO is theoretically embeddable, but suffers from a performance overhead */
		2936
		2937	/* EVBACKEND_IOURING is practically embeddable, but the current implementation is not
		2938	* because our backend_fd is the epoll fd we need as fallback.
		2939	* if the kernel ever is fixed, this might change...
		2940	*/
		2941
2186	return flags;	2942	return flags;
2187	}	2943	}
2188		2944
2189	unsigned int	2945	unsigned int
2190	ev_backend (EV_P) EV_THROW	2946	ev_backend (EV_P) EV_NOEXCEPT
2191	{	2947	{
2192	return backend;	2948	return backend;
2193	}	2949	}
2194		2950
2195	#if EV_FEATURE_API	2951	#if EV_FEATURE_API
2196	unsigned int	2952	unsigned int
2197	ev_iteration (EV_P) EV_THROW	2953	ev_iteration (EV_P) EV_NOEXCEPT
2198	{	2954	{
2199	return loop_count;	2955	return loop_count;
2200	}	2956	}
2201		2957
2202	unsigned int	2958	unsigned int
2203	ev_depth (EV_P) EV_THROW	2959	ev_depth (EV_P) EV_NOEXCEPT
2204	{	2960	{
2205	return loop_depth;	2961	return loop_depth;
2206	}	2962	}
2207		2963
2208	void	2964	void
2209	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2965	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2210	{	2966	{
2211	io_blocktime = interval;	2967	io_blocktime = interval;
2212	}	2968	}
2213		2969
2214	void	2970	void
2215	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2971	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2216	{	2972	{
2217	timeout_blocktime = interval;	2973	timeout_blocktime = interval;
2218	}	2974	}
2219		2975
2220	void	2976	void
2221	ev_set_userdata (EV_P_ void *data) EV_THROW	2977	ev_set_userdata (EV_P_ void *data) EV_NOEXCEPT
2222	{	2978	{
2223	userdata = data;	2979	userdata = data;
2224	}	2980	}
2225		2981
2226	void *	2982	void *
2227	ev_userdata (EV_P) EV_THROW	2983	ev_userdata (EV_P) EV_NOEXCEPT
2228	{	2984	{
2229	return userdata;	2985	return userdata;
2230	}	2986	}
2231		2987
2232	void	2988	void
2233	ev_set_invoke_pending_cb (EV_P_ void (*invoke_pending_cb)(EV_P)) EV_THROW	2989	ev_set_invoke_pending_cb (EV_P_ ev_loop_callback invoke_pending_cb) EV_NOEXCEPT
2234	{	2990	{
2235	invoke_cb = invoke_pending_cb;	2991	invoke_cb = invoke_pending_cb;
2236	}	2992	}
2237		2993
2238	void	2994	void
2239	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_THROW, void (*acquire)(EV_P) EV_THROW) EV_THROW	2995	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_NOEXCEPT, void (*acquire)(EV_P) EV_NOEXCEPT) EV_NOEXCEPT
2240	{	2996	{
2241	release_cb = release;	2997	release_cb = release;
2242	acquire_cb = acquire;	2998	acquire_cb = acquire;
2243	}	2999	}
2244	#endif	3000	#endif
2245		3001
2246	/* initialise a loop structure, must be zero-initialised */	3002	/* initialise a loop structure, must be zero-initialised */
2247	static void noinline ecb_cold	3003	ecb_noinline ecb_cold
		3004	static void
2248	loop_init (EV_P_ unsigned int flags) EV_THROW	3005	loop_init (EV_P_ unsigned int flags) EV_NOEXCEPT
2249	{	3006	{
2250	if (!backend)	3007	if (!backend)
2251	{	3008	{
2252	origflags = flags;	3009	origflags = flags;
2253		3010
…		…
2298	#if EV_ASYNC_ENABLE	3055	#if EV_ASYNC_ENABLE
2299	async_pending = 0;	3056	async_pending = 0;
2300	#endif	3057	#endif
2301	pipe_write_skipped = 0;	3058	pipe_write_skipped = 0;
2302	pipe_write_wanted = 0;	3059	pipe_write_wanted = 0;
		3060	evpipe [0] = -1;
		3061	evpipe [1] = -1;
2303	#if EV_USE_INOTIFY	3062	#if EV_USE_INOTIFY
2304	fs_fd = flags & EVFLAG_NOINOTIFY ? -1 : -2;	3063	fs_fd = flags & EVFLAG_NOINOTIFY ? -1 : -2;
2305	#endif	3064	#endif
2306	#if EV_USE_SIGNALFD	3065	#if EV_USE_SIGNALFD
2307	sigfd = flags & EVFLAG_SIGNALFD ? -2 : -1;	3066	sigfd = flags & EVFLAG_SIGNALFD ? -2 : -1;
…		…
2309		3068
2310	if (!(flags & EVBACKEND_MASK))	3069	if (!(flags & EVBACKEND_MASK))
2311	flags |= ev_recommended_backends ();	3070	flags |= ev_recommended_backends ();
2312		3071
2313	#if EV_USE_IOCP	3072	#if EV_USE_IOCP
2314	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);	3073	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);
2315	#endif	3074	#endif
2316	#if EV_USE_PORT	3075	#if EV_USE_PORT
2317	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);	3076	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);
2318	#endif	3077	#endif
2319	#if EV_USE_KQUEUE	3078	#if EV_USE_KQUEUE
2320	if (!backend && (flags & EVBACKEND_KQUEUE)) backend = kqueue_init (EV_A_ flags);	3079	if (!backend && (flags & EVBACKEND_KQUEUE )) backend = kqueue_init (EV_A_ flags);
		3080	#endif
		3081	#if EV_USE_IOURING
		3082	if (!backend && (flags & EVBACKEND_IOURING )) backend = iouring_init (EV_A_ flags);
		3083	#endif
		3084	#if EV_USE_LINUXAIO
		3085	if (!backend && (flags & EVBACKEND_LINUXAIO)) backend = linuxaio_init (EV_A_ flags);
2321	#endif	3086	#endif
2322	#if EV_USE_EPOLL	3087	#if EV_USE_EPOLL
2323	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);	3088	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);
2324	#endif	3089	#endif
2325	#if EV_USE_POLL	3090	#if EV_USE_POLL
2326	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);	3091	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);
2327	#endif	3092	#endif
2328	#if EV_USE_SELECT	3093	#if EV_USE_SELECT
2329	if (!backend && (flags & EVBACKEND_SELECT)) backend = select_init (EV_A_ flags);	3094	if (!backend && (flags & EVBACKEND_SELECT )) backend = select_init (EV_A_ flags);
2330	#endif	3095	#endif
2331		3096
2332	ev_prepare_init (&pending_w, pendingcb);	3097	ev_prepare_init (&pending_w, pendingcb);
2333		3098
2334	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	3099	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
…		…
2337	#endif	3102	#endif
2338	}	3103	}
2339	}	3104	}
2340		3105
2341	/* free up a loop structure */	3106	/* free up a loop structure */
2342	void ecb_cold	3107	ecb_cold
		3108	void
2343	ev_loop_destroy (EV_P)	3109	ev_loop_destroy (EV_P)
2344	{	3110	{
2345	int i;	3111	int i;
2346		3112
2347	#if EV_MULTIPLICITY	3113	#if EV_MULTIPLICITY
…		…
2350	return;	3116	return;
2351	#endif	3117	#endif
2352		3118
2353	#if EV_CLEANUP_ENABLE	3119	#if EV_CLEANUP_ENABLE
2354	/* queue cleanup watchers (and execute them) */	3120	/* queue cleanup watchers (and execute them) */
2355	if (expect_false (cleanupcnt))	3121	if (ecb_expect_false (cleanupcnt))
2356	{	3122	{
2357	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);	3123	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);
2358	EV_INVOKE_PENDING;	3124	EV_INVOKE_PENDING;
2359	}	3125	}
2360	#endif	3126	#endif
2361		3127
2362	#if EV_CHILD_ENABLE	3128	#if EV_CHILD_ENABLE
2363	if (ev_is_active (&childev))	3129	if (ev_is_default_loop (EV_A) && ev_is_active (&childev))
2364	{	3130	{
2365	ev_ref (EV_A); /* child watcher */	3131	ev_ref (EV_A); /* child watcher */
2366	ev_signal_stop (EV_A_ &childev);	3132	ev_signal_stop (EV_A_ &childev);
2367	}	3133	}
2368	#endif	3134	#endif
…		…
2370	if (ev_is_active (&pipe_w))	3136	if (ev_is_active (&pipe_w))
2371	{	3137	{
2372	/*ev_ref (EV_A);*/	3138	/*ev_ref (EV_A);*/
2373	/*ev_io_stop (EV_A_ &pipe_w);*/	3139	/*ev_io_stop (EV_A_ &pipe_w);*/
2374		3140
2375	#if EV_USE_EVENTFD
2376	if (evfd >= 0)
2377	close (evfd);
2378	#endif
2379
2380	if (evpipe [0] >= 0)
2381	{
2382	EV_WIN32_CLOSE_FD (evpipe [0]);	3141	if (evpipe [0] >= 0) EV_WIN32_CLOSE_FD (evpipe [0]);
2383	EV_WIN32_CLOSE_FD (evpipe [1]);	3142	if (evpipe [1] >= 0) EV_WIN32_CLOSE_FD (evpipe [1]);
2384	}
2385	}	3143	}
2386		3144
2387	#if EV_USE_SIGNALFD	3145	#if EV_USE_SIGNALFD
2388	if (ev_is_active (&sigfd_w))	3146	if (ev_is_active (&sigfd_w))
2389	close (sigfd);	3147	close (sigfd);
…		…
2396		3154
2397	if (backend_fd >= 0)	3155	if (backend_fd >= 0)
2398	close (backend_fd);	3156	close (backend_fd);
2399		3157
2400	#if EV_USE_IOCP	3158	#if EV_USE_IOCP
2401	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);	3159	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);
2402	#endif	3160	#endif
2403	#if EV_USE_PORT	3161	#if EV_USE_PORT
2404	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);	3162	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);
2405	#endif	3163	#endif
2406	#if EV_USE_KQUEUE	3164	#if EV_USE_KQUEUE
2407	if (backend == EVBACKEND_KQUEUE) kqueue_destroy (EV_A);	3165	if (backend == EVBACKEND_KQUEUE ) kqueue_destroy (EV_A);
		3166	#endif
		3167	#if EV_USE_IOURING
		3168	if (backend == EVBACKEND_IOURING ) iouring_destroy (EV_A);
		3169	#endif
		3170	#if EV_USE_LINUXAIO
		3171	if (backend == EVBACKEND_LINUXAIO) linuxaio_destroy (EV_A);
2408	#endif	3172	#endif
2409	#if EV_USE_EPOLL	3173	#if EV_USE_EPOLL
2410	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);	3174	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);
2411	#endif	3175	#endif
2412	#if EV_USE_POLL	3176	#if EV_USE_POLL
2413	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);	3177	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);
2414	#endif	3178	#endif
2415	#if EV_USE_SELECT	3179	#if EV_USE_SELECT
2416	if (backend == EVBACKEND_SELECT) select_destroy (EV_A);	3180	if (backend == EVBACKEND_SELECT ) select_destroy (EV_A);
2417	#endif	3181	#endif
2418		3182
2419	for (i = NUMPRI; i--; )	3183	for (i = NUMPRI; i--; )
2420	{	3184	{
2421	array_free (pending, [i]);	3185	array_free (pending, [i]);
…		…
2463		3227
2464	inline_size void	3228	inline_size void
2465	loop_fork (EV_P)	3229	loop_fork (EV_P)
2466	{	3230	{
2467	#if EV_USE_PORT	3231	#if EV_USE_PORT
2468	if (backend == EVBACKEND_PORT ) port_fork (EV_A);	3232	if (backend == EVBACKEND_PORT ) port_fork (EV_A);
2469	#endif	3233	#endif
2470	#if EV_USE_KQUEUE	3234	#if EV_USE_KQUEUE
2471	if (backend == EVBACKEND_KQUEUE) kqueue_fork (EV_A);	3235	if (backend == EVBACKEND_KQUEUE ) kqueue_fork (EV_A);
		3236	#endif
		3237	#if EV_USE_IOURING
		3238	if (backend == EVBACKEND_IOURING ) iouring_fork (EV_A);
		3239	#endif
		3240	#if EV_USE_LINUXAIO
		3241	if (backend == EVBACKEND_LINUXAIO) linuxaio_fork (EV_A);
2472	#endif	3242	#endif
2473	#if EV_USE_EPOLL	3243	#if EV_USE_EPOLL
2474	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);	3244	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);
2475	#endif	3245	#endif
2476	#if EV_USE_INOTIFY	3246	#if EV_USE_INOTIFY
2477	infy_fork (EV_A);	3247	infy_fork (EV_A);
2478	#endif	3248	#endif
2479		3249
		3250	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2480	if (ev_is_active (&pipe_w))	3251	if (ev_is_active (&pipe_w) && postfork != 2)
2481	{	3252	{
2482	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */	3253	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */
2483		3254
2484	ev_ref (EV_A);	3255	ev_ref (EV_A);
2485	ev_io_stop (EV_A_ &pipe_w);	3256	ev_io_stop (EV_A_ &pipe_w);
2486		3257
2487	#if EV_USE_EVENTFD
2488	if (evfd >= 0)
2489	close (evfd);
2490	#endif
2491
2492	if (evpipe [0] >= 0)	3258	if (evpipe [0] >= 0)
2493	{
2494	EV_WIN32_CLOSE_FD (evpipe [0]);	3259	EV_WIN32_CLOSE_FD (evpipe [0]);
2495	EV_WIN32_CLOSE_FD (evpipe [1]);
2496	}
2497		3260
2498	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2499	evpipe_init (EV_A);	3261	evpipe_init (EV_A);
2500	/* now iterate over everything, in case we missed something */	3262	/* iterate over everything, in case we missed something before */
2501	pipecb (EV_A_ &pipe_w, EV_READ);	3263	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);
2502	#endif
2503	}	3264	}
		3265	#endif
2504		3266
2505	postfork = 0;	3267	postfork = 0;
2506	}	3268	}
2507		3269
2508	#if EV_MULTIPLICITY	3270	#if EV_MULTIPLICITY
2509		3271
		3272	ecb_cold
2510	struct ev_loop * ecb_cold	3273	struct ev_loop *
2511	ev_loop_new (unsigned int flags) EV_THROW	3274	ev_loop_new (unsigned int flags) EV_NOEXCEPT
2512	{	3275	{
2513	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));	3276	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));
2514		3277
2515	memset (EV_A, 0, sizeof (struct ev_loop));	3278	memset (EV_A, 0, sizeof (struct ev_loop));
2516	loop_init (EV_A_ flags);	3279	loop_init (EV_A_ flags);
…		…
2523	}	3286	}
2524		3287
2525	#endif /* multiplicity */	3288	#endif /* multiplicity */
2526		3289
2527	#if EV_VERIFY	3290	#if EV_VERIFY
2528	static void noinline ecb_cold	3291	ecb_noinline ecb_cold
		3292	static void
2529	verify_watcher (EV_P_ W w)	3293	verify_watcher (EV_P_ W w)
2530	{	3294	{
2531	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));	3295	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));
2532		3296
2533	if (w->pending)	3297	if (w->pending)
2534	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));	3298	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));
2535	}	3299	}
2536		3300
2537	static void noinline ecb_cold	3301	ecb_noinline ecb_cold
		3302	static void
2538	verify_heap (EV_P_ ANHE *heap, int N)	3303	verify_heap (EV_P_ ANHE *heap, int N)
2539	{	3304	{
2540	int i;	3305	int i;
2541		3306
2542	for (i = HEAP0; i < N + HEAP0; ++i)	3307	for (i = HEAP0; i < N + HEAP0; ++i)
…		…
2547		3312
2548	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));	3313	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));
2549	}	3314	}
2550	}	3315	}
2551		3316
2552	static void noinline ecb_cold	3317	ecb_noinline ecb_cold
		3318	static void
2553	array_verify (EV_P_ W *ws, int cnt)	3319	array_verify (EV_P_ W *ws, int cnt)
2554	{	3320	{
2555	while (cnt--)	3321	while (cnt--)
2556	{	3322	{
2557	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));	3323	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));
…		…
2560	}	3326	}
2561	#endif	3327	#endif
2562		3328
2563	#if EV_FEATURE_API	3329	#if EV_FEATURE_API
2564	void ecb_cold	3330	void ecb_cold
2565	ev_verify (EV_P) EV_THROW	3331	ev_verify (EV_P) EV_NOEXCEPT
2566	{	3332	{
2567	#if EV_VERIFY	3333	#if EV_VERIFY
2568	int i;	3334	int i;
2569	WL w, w2;	3335	WL w, w2;
2570		3336
…		…
2646	#endif	3412	#endif
2647	}	3413	}
2648	#endif	3414	#endif
2649		3415
2650	#if EV_MULTIPLICITY	3416	#if EV_MULTIPLICITY
		3417	ecb_cold
2651	struct ev_loop * ecb_cold	3418	struct ev_loop *
2652	#else	3419	#else
2653	int	3420	int
2654	#endif	3421	#endif
2655	ev_default_loop (unsigned int flags) EV_THROW	3422	ev_default_loop (unsigned int flags) EV_NOEXCEPT
2656	{	3423	{
2657	if (!ev_default_loop_ptr)	3424	if (!ev_default_loop_ptr)
2658	{	3425	{
2659	#if EV_MULTIPLICITY	3426	#if EV_MULTIPLICITY
2660	EV_P = ev_default_loop_ptr = &default_loop_struct;	3427	EV_P = ev_default_loop_ptr = &default_loop_struct;
…		…
2679		3446
2680	return ev_default_loop_ptr;	3447	return ev_default_loop_ptr;
2681	}	3448	}
2682		3449
2683	void	3450	void
2684	ev_loop_fork (EV_P) EV_THROW	3451	ev_loop_fork (EV_P) EV_NOEXCEPT
2685	{	3452	{
2686	postfork = 1; /* must be in line with ev_default_fork */	3453	postfork = 1;
2687	}	3454	}
2688		3455
2689	/*****************************************************************************/	3456	/*****************************************************************************/
2690		3457
2691	void	3458	void
…		…
2693	{	3460	{
2694	EV_CB_INVOKE ((W)w, revents);	3461	EV_CB_INVOKE ((W)w, revents);
2695	}	3462	}
2696		3463
2697	unsigned int	3464	unsigned int
2698	ev_pending_count (EV_P) EV_THROW	3465	ev_pending_count (EV_P) EV_NOEXCEPT
2699	{	3466	{
2700	int pri;	3467	int pri;
2701	unsigned int count = 0;	3468	unsigned int count = 0;
2702		3469
2703	for (pri = NUMPRI; pri--; )	3470	for (pri = NUMPRI; pri--; )
2704	count += pendingcnt [pri];	3471	count += pendingcnt [pri];
2705		3472
2706	return count;	3473	return count;
2707	}	3474	}
2708		3475
2709	void noinline	3476	ecb_noinline
		3477	void
2710	ev_invoke_pending (EV_P)	3478	ev_invoke_pending (EV_P)
2711	{	3479	{
2712	for (pendingpri = NUMPRI; pendingpri--; ) /* pendingpri is modified during the loop */	3480	pendingpri = NUMPRI;
		3481
		3482	do
		3483	{
		3484	--pendingpri;
		3485
		3486	/* pendingpri possibly gets modified in the inner loop */
2713	while (pendingcnt [pendingpri])	3487	while (pendingcnt [pendingpri])
2714	{	3488	{
2715	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];	3489	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];
2716		3490
2717	p->w->pending = 0;	3491	p->w->pending = 0;
2718	EV_CB_INVOKE (p->w, p->events);	3492	EV_CB_INVOKE (p->w, p->events);
2719	EV_FREQUENT_CHECK;	3493	EV_FREQUENT_CHECK;
2720	}	3494	}
		3495	}
		3496	while (pendingpri);
2721	}	3497	}
2722		3498
2723	#if EV_IDLE_ENABLE	3499	#if EV_IDLE_ENABLE
2724	/* make idle watchers pending. this handles the "call-idle */	3500	/* make idle watchers pending. this handles the "call-idle */
2725	/* only when higher priorities are idle" logic */	3501	/* only when higher priorities are idle" logic */
2726	inline_size void	3502	inline_size void
2727	idle_reify (EV_P)	3503	idle_reify (EV_P)
2728	{	3504	{
2729	if (expect_false (idleall))	3505	if (ecb_expect_false (idleall))
2730	{	3506	{
2731	int pri;	3507	int pri;
2732		3508
2733	for (pri = NUMPRI; pri--; )	3509	for (pri = NUMPRI; pri--; )
2734	{	3510	{
…		…
2783	}	3559	}
2784	}	3560	}
2785		3561
2786	#if EV_PERIODIC_ENABLE	3562	#if EV_PERIODIC_ENABLE
2787		3563
2788	static void noinline	3564	ecb_noinline
		3565	static void
2789	periodic_recalc (EV_P_ ev_periodic *w)	3566	periodic_recalc (EV_P_ ev_periodic *w)
2790	{	3567	{
2791	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;	3568	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;
2792	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);	3569	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);
2793		3570
…		…
2795	while (at <= ev_rt_now)	3572	while (at <= ev_rt_now)
2796	{	3573	{
2797	ev_tstamp nat = at + w->interval;	3574	ev_tstamp nat = at + w->interval;
2798		3575
2799	/* when resolution fails us, we use ev_rt_now */	3576	/* when resolution fails us, we use ev_rt_now */
2800	if (expect_false (nat == at))	3577	if (ecb_expect_false (nat == at))
2801	{	3578	{
2802	at = ev_rt_now;	3579	at = ev_rt_now;
2803	break;	3580	break;
2804	}	3581	}
2805		3582
…		…
2815	{	3592	{
2816	EV_FREQUENT_CHECK;	3593	EV_FREQUENT_CHECK;
2817		3594
2818	while (periodiccnt && ANHE_at (periodics [HEAP0]) < ev_rt_now)	3595	while (periodiccnt && ANHE_at (periodics [HEAP0]) < ev_rt_now)
2819	{	3596	{
2820	int feed_count = 0;
2821
2822	do	3597	do
2823	{	3598	{
2824	ev_periodic *w = (ev_periodic *)ANHE_w (periodics [HEAP0]);	3599	ev_periodic *w = (ev_periodic *)ANHE_w (periodics [HEAP0]);
2825		3600
2826	/*assert (("libev: inactive timer on periodic heap detected", ev_is_active (w)));*/	3601	/*assert (("libev: inactive timer on periodic heap detected", ev_is_active (w)));*/
…		…
2853	}	3628	}
2854	}	3629	}
2855		3630
2856	/* simply recalculate all periodics */	3631	/* simply recalculate all periodics */
2857	/* TODO: maybe ensure that at least one event happens when jumping forward? */	3632	/* TODO: maybe ensure that at least one event happens when jumping forward? */
2858	static void noinline ecb_cold	3633	ecb_noinline ecb_cold
		3634	static void
2859	periodics_reschedule (EV_P)	3635	periodics_reschedule (EV_P)
2860	{	3636	{
2861	int i;	3637	int i;
2862		3638
2863	/* adjust periodics after time jump */	3639	/* adjust periodics after time jump */
…		…
2876	reheap (periodics, periodiccnt);	3652	reheap (periodics, periodiccnt);
2877	}	3653	}
2878	#endif	3654	#endif
2879		3655
2880	/* adjust all timers by a given offset */	3656	/* adjust all timers by a given offset */
2881	static void noinline ecb_cold	3657	ecb_noinline ecb_cold
		3658	static void
2882	timers_reschedule (EV_P_ ev_tstamp adjust)	3659	timers_reschedule (EV_P_ ev_tstamp adjust)
2883	{	3660	{
2884	int i;	3661	int i;
2885		3662
2886	for (i = 0; i < timercnt; ++i)	3663	for (i = 0; i < timercnt; ++i)
…		…
2895	/* also detect if there was a timejump, and act accordingly */	3672	/* also detect if there was a timejump, and act accordingly */
2896	inline_speed void	3673	inline_speed void
2897	time_update (EV_P_ ev_tstamp max_block)	3674	time_update (EV_P_ ev_tstamp max_block)
2898	{	3675	{
2899	#if EV_USE_MONOTONIC	3676	#if EV_USE_MONOTONIC
2900	if (expect_true (have_monotonic))	3677	if (ecb_expect_true (have_monotonic))
2901	{	3678	{
2902	int i;	3679	int i;
2903	ev_tstamp odiff = rtmn_diff;	3680	ev_tstamp odiff = rtmn_diff;
2904		3681
2905	mn_now = get_clock ();	3682	mn_now = get_clock ();
2906		3683
2907	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */	3684	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */
2908	/* interpolate in the meantime */	3685	/* interpolate in the meantime */
2909	if (expect_true (mn_now - now_floor < MIN_TIMEJUMP * .5))	3686	if (ecb_expect_true (mn_now - now_floor < MIN_TIMEJUMP * .5))
2910	{	3687	{
2911	ev_rt_now = rtmn_diff + mn_now;	3688	ev_rt_now = rtmn_diff + mn_now;
2912	return;	3689	return;
2913	}	3690	}
2914		3691
…		…
2928	ev_tstamp diff;	3705	ev_tstamp diff;
2929	rtmn_diff = ev_rt_now - mn_now;	3706	rtmn_diff = ev_rt_now - mn_now;
2930		3707
2931	diff = odiff - rtmn_diff;	3708	diff = odiff - rtmn_diff;
2932		3709
2933	if (expect_true ((diff < 0. ? -diff : diff) < MIN_TIMEJUMP))	3710	if (ecb_expect_true ((diff < 0. ? -diff : diff) < MIN_TIMEJUMP))
2934	return; /* all is well */	3711	return; /* all is well */
2935		3712
2936	ev_rt_now = ev_time ();	3713	ev_rt_now = ev_time ();
2937	mn_now = get_clock ();	3714	mn_now = get_clock ();
2938	now_floor = mn_now;	3715	now_floor = mn_now;
…		…
2947	else	3724	else
2948	#endif	3725	#endif
2949	{	3726	{
2950	ev_rt_now = ev_time ();	3727	ev_rt_now = ev_time ();
2951		3728
2952	if (expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + MIN_TIMEJUMP))	3729	if (ecb_expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + MIN_TIMEJUMP))
2953	{	3730	{
2954	/* adjust timers. this is easy, as the offset is the same for all of them */	3731	/* adjust timers. this is easy, as the offset is the same for all of them */
2955	timers_reschedule (EV_A_ ev_rt_now - mn_now);	3732	timers_reschedule (EV_A_ ev_rt_now - mn_now);
2956	#if EV_PERIODIC_ENABLE	3733	#if EV_PERIODIC_ENABLE
2957	periodics_reschedule (EV_A);	3734	periodics_reschedule (EV_A);
…		…
2980	#if EV_VERIFY >= 2	3757	#if EV_VERIFY >= 2
2981	ev_verify (EV_A);	3758	ev_verify (EV_A);
2982	#endif	3759	#endif
2983		3760
2984	#ifndef _WIN32	3761	#ifndef _WIN32
2985	if (expect_false (curpid)) /* penalise the forking check even more */	3762	if (ecb_expect_false (curpid)) /* penalise the forking check even more */
2986	if (expect_false (getpid () != curpid))	3763	if (ecb_expect_false (getpid () != curpid))
2987	{	3764	{
2988	curpid = getpid ();	3765	curpid = getpid ();
2989	postfork = 1;	3766	postfork = 1;
2990	}	3767	}
2991	#endif	3768	#endif
2992		3769
2993	#if EV_FORK_ENABLE	3770	#if EV_FORK_ENABLE
2994	/* we might have forked, so queue fork handlers */	3771	/* we might have forked, so queue fork handlers */
2995	if (expect_false (postfork))	3772	if (ecb_expect_false (postfork))
2996	if (forkcnt)	3773	if (forkcnt)
2997	{	3774	{
2998	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);	3775	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);
2999	EV_INVOKE_PENDING;	3776	EV_INVOKE_PENDING;
3000	}	3777	}
3001	#endif	3778	#endif
3002		3779
3003	#if EV_PREPARE_ENABLE	3780	#if EV_PREPARE_ENABLE
3004	/* queue prepare watchers (and execute them) */	3781	/* queue prepare watchers (and execute them) */
3005	if (expect_false (preparecnt))	3782	if (ecb_expect_false (preparecnt))
3006	{	3783	{
3007	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);	3784	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);
3008	EV_INVOKE_PENDING;	3785	EV_INVOKE_PENDING;
3009	}	3786	}
3010	#endif	3787	#endif
3011		3788
3012	if (expect_false (loop_done))	3789	if (ecb_expect_false (loop_done))
3013	break;	3790	break;
3014		3791
3015	/* we might have forked, so reify kernel state if necessary */	3792	/* we might have forked, so reify kernel state if necessary */
3016	if (expect_false (postfork))	3793	if (ecb_expect_false (postfork))
3017	loop_fork (EV_A);	3794	loop_fork (EV_A);
3018		3795
3019	/* update fd-related kernel structures */	3796	/* update fd-related kernel structures */
3020	fd_reify (EV_A);	3797	fd_reify (EV_A);
3021		3798
…		…
3033	/* from now on, we want a pipe-wake-up */	3810	/* from now on, we want a pipe-wake-up */
3034	pipe_write_wanted = 1;	3811	pipe_write_wanted = 1;
3035		3812
3036	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */	3813	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */
3037		3814
3038	if (expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))	3815	if (ecb_expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))
3039	{	3816	{
3040	waittime = MAX_BLOCKTIME;	3817	waittime = MAX_BLOCKTIME;
3041		3818
3042	if (timercnt)	3819	if (timercnt)
3043	{	3820	{
…		…
3052	if (waittime > to) waittime = to;	3829	if (waittime > to) waittime = to;
3053	}	3830	}
3054	#endif	3831	#endif
3055		3832
3056	/* don't let timeouts decrease the waittime below timeout_blocktime */	3833	/* don't let timeouts decrease the waittime below timeout_blocktime */
3057	if (expect_false (waittime < timeout_blocktime))	3834	if (ecb_expect_false (waittime < timeout_blocktime))
3058	waittime = timeout_blocktime;	3835	waittime = timeout_blocktime;
3059		3836
3060	/* at this point, we NEED to wait, so we have to ensure */	3837	/* at this point, we NEED to wait, so we have to ensure */
3061	/* to pass a minimum nonzero value to the backend */	3838	/* to pass a minimum nonzero value to the backend */
3062	if (expect_false (waittime < backend_mintime))	3839	if (ecb_expect_false (waittime < backend_mintime))
3063	waittime = backend_mintime;	3840	waittime = backend_mintime;
3064		3841
3065	/* extra check because io_blocktime is commonly 0 */	3842	/* extra check because io_blocktime is commonly 0 */
3066	if (expect_false (io_blocktime))	3843	if (ecb_expect_false (io_blocktime))
3067	{	3844	{
3068	sleeptime = io_blocktime - (mn_now - prev_mn_now);	3845	sleeptime = io_blocktime - (mn_now - prev_mn_now);
3069		3846
3070	if (sleeptime > waittime - backend_mintime)	3847	if (sleeptime > waittime - backend_mintime)
3071	sleeptime = waittime - backend_mintime;	3848	sleeptime = waittime - backend_mintime;
3072		3849
3073	if (expect_true (sleeptime > 0.))	3850	if (ecb_expect_true (sleeptime > 0.))
3074	{	3851	{
3075	ev_sleep (sleeptime);	3852	ev_sleep (sleeptime);
3076	waittime -= sleeptime;	3853	waittime -= sleeptime;
3077	}	3854	}
3078	}	3855	}
…		…
3085	backend_poll (EV_A_ waittime);	3862	backend_poll (EV_A_ waittime);
3086	assert ((loop_done = EVBREAK_CANCEL, 1)); /* assert for side effect */	3863	assert ((loop_done = EVBREAK_CANCEL, 1)); /* assert for side effect */
3087		3864
3088	pipe_write_wanted = 0; /* just an optimisation, no fence needed */	3865	pipe_write_wanted = 0; /* just an optimisation, no fence needed */
3089		3866
		3867	ECB_MEMORY_FENCE_ACQUIRE;
3090	if (pipe_write_skipped)	3868	if (pipe_write_skipped)
3091	{	3869	{
3092	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));	3870	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));
3093	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);	3871	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);
3094	}	3872	}
3095		3873
3096
3097	/* update ev_rt_now, do magic */	3874	/* update ev_rt_now, do magic */
3098	time_update (EV_A_ waittime + sleeptime);	3875	time_update (EV_A_ waittime + sleeptime);
3099	}	3876	}
3100		3877
3101	/* queue pending timers and reschedule them */	3878	/* queue pending timers and reschedule them */
…		…
3109	idle_reify (EV_A);	3886	idle_reify (EV_A);
3110	#endif	3887	#endif
3111		3888
3112	#if EV_CHECK_ENABLE	3889	#if EV_CHECK_ENABLE
3113	/* queue check watchers, to be executed first */	3890	/* queue check watchers, to be executed first */
3114	if (expect_false (checkcnt))	3891	if (ecb_expect_false (checkcnt))
3115	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);	3892	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);
3116	#endif	3893	#endif
3117		3894
3118	EV_INVOKE_PENDING;	3895	EV_INVOKE_PENDING;
3119	}	3896	}
3120	while (expect_true (	3897	while (ecb_expect_true (
3121	activecnt	3898	activecnt
3122	&& !loop_done	3899	&& !loop_done
3123	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))	3900	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))
3124	));	3901	));
3125		3902
…		…
3132		3909
3133	return activecnt;	3910	return activecnt;
3134	}	3911	}
3135		3912
3136	void	3913	void
3137	ev_break (EV_P_ int how) EV_THROW	3914	ev_break (EV_P_ int how) EV_NOEXCEPT
3138	{	3915	{
3139	loop_done = how;	3916	loop_done = how;
3140	}	3917	}
3141		3918
3142	void	3919	void
3143	ev_ref (EV_P) EV_THROW	3920	ev_ref (EV_P) EV_NOEXCEPT
3144	{	3921	{
3145	++activecnt;	3922	++activecnt;
3146	}	3923	}
3147		3924
3148	void	3925	void
3149	ev_unref (EV_P) EV_THROW	3926	ev_unref (EV_P) EV_NOEXCEPT
3150	{	3927	{
3151	--activecnt;	3928	--activecnt;
3152	}	3929	}
3153		3930
3154	void	3931	void
3155	ev_now_update (EV_P) EV_THROW	3932	ev_now_update (EV_P) EV_NOEXCEPT
3156	{	3933	{
3157	time_update (EV_A_ 1e100);	3934	time_update (EV_A_ 1e100);
3158	}	3935	}
3159		3936
3160	void	3937	void
3161	ev_suspend (EV_P) EV_THROW	3938	ev_suspend (EV_P) EV_NOEXCEPT
3162	{	3939	{
3163	ev_now_update (EV_A);	3940	ev_now_update (EV_A);
3164	}	3941	}
3165		3942
3166	void	3943	void
3167	ev_resume (EV_P) EV_THROW	3944	ev_resume (EV_P) EV_NOEXCEPT
3168	{	3945	{
3169	ev_tstamp mn_prev = mn_now;	3946	ev_tstamp mn_prev = mn_now;
3170		3947
3171	ev_now_update (EV_A);	3948	ev_now_update (EV_A);
3172	timers_reschedule (EV_A_ mn_now - mn_prev);	3949	timers_reschedule (EV_A_ mn_now - mn_prev);
…		…
3189	inline_size void	3966	inline_size void
3190	wlist_del (WL *head, WL elem)	3967	wlist_del (WL *head, WL elem)
3191	{	3968	{
3192	while (*head)	3969	while (*head)
3193	{	3970	{
3194	if (expect_true (*head == elem))	3971	if (ecb_expect_true (*head == elem))
3195	{	3972	{
3196	*head = elem->next;	3973	*head = elem->next;
3197	break;	3974	break;
3198	}	3975	}
3199		3976
…		…
3211	w->pending = 0;	3988	w->pending = 0;
3212	}	3989	}
3213	}	3990	}
3214		3991
3215	int	3992	int
3216	ev_clear_pending (EV_P_ void *w) EV_THROW	3993	ev_clear_pending (EV_P_ void *w) EV_NOEXCEPT
3217	{	3994	{
3218	W w_ = (W)w;	3995	W w_ = (W)w;
3219	int pending = w_->pending;	3996	int pending = w_->pending;
3220		3997
3221	if (expect_true (pending))	3998	if (ecb_expect_true (pending))
3222	{	3999	{
3223	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;	4000	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;
3224	p->w = (W)&pending_w;	4001	p->w = (W)&pending_w;
3225	w_->pending = 0;	4002	w_->pending = 0;
3226	return p->events;	4003	return p->events;
…		…
3253	w->active = 0;	4030	w->active = 0;
3254	}	4031	}
3255		4032
3256	/*****************************************************************************/	4033	/*****************************************************************************/
3257		4034
3258	void noinline	4035	ecb_noinline
		4036	void
3259	ev_io_start (EV_P_ ev_io *w) EV_THROW	4037	ev_io_start (EV_P_ ev_io *w) EV_NOEXCEPT
3260	{	4038	{
3261	int fd = w->fd;	4039	int fd = w->fd;
3262		4040
3263	if (expect_false (ev_is_active (w)))	4041	if (ecb_expect_false (ev_is_active (w)))
3264	return;	4042	return;
3265		4043
3266	assert (("libev: ev_io_start called with negative fd", fd >= 0));	4044	assert (("libev: ev_io_start called with negative fd", fd >= 0));
3267	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));	4045	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));
3268		4046
		4047	#if EV_VERIFY >= 2
		4048	assert (("libev: ev_io_start called on watcher with invalid fd", fd_valid (fd)));
		4049	#endif
3269	EV_FREQUENT_CHECK;	4050	EV_FREQUENT_CHECK;
3270		4051
3271	ev_start (EV_A_ (W)w, 1);	4052	ev_start (EV_A_ (W)w, 1);
3272	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_init_zero);	4053	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_needsize_zerofill);
3273	wlist_add (&anfds[fd].head, (WL)w);	4054	wlist_add (&anfds[fd].head, (WL)w);
3274		4055
3275	/* common bug, apparently */	4056	/* common bug, apparently */
3276	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));	4057	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));
3277		4058
…		…
3279	w->events &= ~EV__IOFDSET;	4060	w->events &= ~EV__IOFDSET;
3280		4061
3281	EV_FREQUENT_CHECK;	4062	EV_FREQUENT_CHECK;
3282	}	4063	}
3283		4064
3284	void noinline	4065	ecb_noinline
		4066	void
3285	ev_io_stop (EV_P_ ev_io *w) EV_THROW	4067	ev_io_stop (EV_P_ ev_io *w) EV_NOEXCEPT
3286	{	4068	{
3287	clear_pending (EV_A_ (W)w);	4069	clear_pending (EV_A_ (W)w);
3288	if (expect_false (!ev_is_active (w)))	4070	if (ecb_expect_false (!ev_is_active (w)))
3289	return;	4071	return;
3290		4072
3291	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));	4073	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));
3292		4074
		4075	#if EV_VERIFY >= 2
		4076	assert (("libev: ev_io_stop called on watcher with invalid fd", fd_valid (w->fd)));
		4077	#endif
3293	EV_FREQUENT_CHECK;	4078	EV_FREQUENT_CHECK;
3294		4079
3295	wlist_del (&anfds[w->fd].head, (WL)w);	4080	wlist_del (&anfds[w->fd].head, (WL)w);
3296	ev_stop (EV_A_ (W)w);	4081	ev_stop (EV_A_ (W)w);
3297		4082
3298	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);	4083	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);
3299		4084
3300	EV_FREQUENT_CHECK;	4085	EV_FREQUENT_CHECK;
3301	}	4086	}
3302		4087
3303	void noinline	4088	ecb_noinline
		4089	void
3304	ev_timer_start (EV_P_ ev_timer *w) EV_THROW	4090	ev_timer_start (EV_P_ ev_timer *w) EV_NOEXCEPT
3305	{	4091	{
3306	if (expect_false (ev_is_active (w)))	4092	if (ecb_expect_false (ev_is_active (w)))
3307	return;	4093	return;
3308		4094
3309	ev_at (w) += mn_now;	4095	ev_at (w) += mn_now;
3310		4096
3311	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));	4097	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));
3312		4098
3313	EV_FREQUENT_CHECK;	4099	EV_FREQUENT_CHECK;
3314		4100
3315	++timercnt;	4101	++timercnt;
3316	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);	4102	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);
3317	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, EMPTY2);	4103	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, array_needsize_noinit);
3318	ANHE_w (timers [ev_active (w)]) = (WT)w;	4104	ANHE_w (timers [ev_active (w)]) = (WT)w;
3319	ANHE_at_cache (timers [ev_active (w)]);	4105	ANHE_at_cache (timers [ev_active (w)]);
3320	upheap (timers, ev_active (w));	4106	upheap (timers, ev_active (w));
3321		4107
3322	EV_FREQUENT_CHECK;	4108	EV_FREQUENT_CHECK;
3323		4109
3324	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/	4110	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/
3325	}	4111	}
3326		4112
3327	void noinline	4113	ecb_noinline
		4114	void
3328	ev_timer_stop (EV_P_ ev_timer *w) EV_THROW	4115	ev_timer_stop (EV_P_ ev_timer *w) EV_NOEXCEPT
3329	{	4116	{
3330	clear_pending (EV_A_ (W)w);	4117	clear_pending (EV_A_ (W)w);
3331	if (expect_false (!ev_is_active (w)))	4118	if (ecb_expect_false (!ev_is_active (w)))
3332	return;	4119	return;
3333		4120
3334	EV_FREQUENT_CHECK;	4121	EV_FREQUENT_CHECK;
3335		4122
3336	{	4123	{
…		…
3338		4125
3339	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));	4126	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));
3340		4127
3341	--timercnt;	4128	--timercnt;
3342		4129
3343	if (expect_true (active < timercnt + HEAP0))	4130	if (ecb_expect_true (active < timercnt + HEAP0))
3344	{	4131	{
3345	timers [active] = timers [timercnt + HEAP0];	4132	timers [active] = timers [timercnt + HEAP0];
3346	adjustheap (timers, timercnt, active);	4133	adjustheap (timers, timercnt, active);
3347	}	4134	}
3348	}	4135	}
…		…
3352	ev_stop (EV_A_ (W)w);	4139	ev_stop (EV_A_ (W)w);
3353		4140
3354	EV_FREQUENT_CHECK;	4141	EV_FREQUENT_CHECK;
3355	}	4142	}
3356		4143
3357	void noinline	4144	ecb_noinline
		4145	void
3358	ev_timer_again (EV_P_ ev_timer *w) EV_THROW	4146	ev_timer_again (EV_P_ ev_timer *w) EV_NOEXCEPT
3359	{	4147	{
3360	EV_FREQUENT_CHECK;	4148	EV_FREQUENT_CHECK;
3361		4149
3362	clear_pending (EV_A_ (W)w);	4150	clear_pending (EV_A_ (W)w);
3363		4151
…		…
3380		4168
3381	EV_FREQUENT_CHECK;	4169	EV_FREQUENT_CHECK;
3382	}	4170	}
3383		4171
3384	ev_tstamp	4172	ev_tstamp
3385	ev_timer_remaining (EV_P_ ev_timer *w) EV_THROW	4173	ev_timer_remaining (EV_P_ ev_timer *w) EV_NOEXCEPT
3386	{	4174	{
3387	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);	4175	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);
3388	}	4176	}
3389		4177
3390	#if EV_PERIODIC_ENABLE	4178	#if EV_PERIODIC_ENABLE
3391	void noinline	4179	ecb_noinline
		4180	void
3392	ev_periodic_start (EV_P_ ev_periodic *w) EV_THROW	4181	ev_periodic_start (EV_P_ ev_periodic *w) EV_NOEXCEPT
3393	{	4182	{
3394	if (expect_false (ev_is_active (w)))	4183	if (ecb_expect_false (ev_is_active (w)))
3395	return;	4184	return;
3396		4185
3397	if (w->reschedule_cb)	4186	if (w->reschedule_cb)
3398	ev_at (w) = w->reschedule_cb (w, ev_rt_now);	4187	ev_at (w) = w->reschedule_cb (w, ev_rt_now);
3399	else if (w->interval)	4188	else if (w->interval)
…		…
3406		4195
3407	EV_FREQUENT_CHECK;	4196	EV_FREQUENT_CHECK;
3408		4197
3409	++periodiccnt;	4198	++periodiccnt;
3410	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);	4199	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);
3411	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, EMPTY2);	4200	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, array_needsize_noinit);
3412	ANHE_w (periodics [ev_active (w)]) = (WT)w;	4201	ANHE_w (periodics [ev_active (w)]) = (WT)w;
3413	ANHE_at_cache (periodics [ev_active (w)]);	4202	ANHE_at_cache (periodics [ev_active (w)]);
3414	upheap (periodics, ev_active (w));	4203	upheap (periodics, ev_active (w));
3415		4204
3416	EV_FREQUENT_CHECK;	4205	EV_FREQUENT_CHECK;
3417		4206
3418	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/	4207	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/
3419	}	4208	}
3420		4209
3421	void noinline	4210	ecb_noinline
		4211	void
3422	ev_periodic_stop (EV_P_ ev_periodic *w) EV_THROW	4212	ev_periodic_stop (EV_P_ ev_periodic *w) EV_NOEXCEPT
3423	{	4213	{
3424	clear_pending (EV_A_ (W)w);	4214	clear_pending (EV_A_ (W)w);
3425	if (expect_false (!ev_is_active (w)))	4215	if (ecb_expect_false (!ev_is_active (w)))
3426	return;	4216	return;
3427		4217
3428	EV_FREQUENT_CHECK;	4218	EV_FREQUENT_CHECK;
3429		4219
3430	{	4220	{
…		…
3432		4222
3433	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));	4223	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));
3434		4224
3435	--periodiccnt;	4225	--periodiccnt;
3436		4226
3437	if (expect_true (active < periodiccnt + HEAP0))	4227	if (ecb_expect_true (active < periodiccnt + HEAP0))
3438	{	4228	{
3439	periodics [active] = periodics [periodiccnt + HEAP0];	4229	periodics [active] = periodics [periodiccnt + HEAP0];
3440	adjustheap (periodics, periodiccnt, active);	4230	adjustheap (periodics, periodiccnt, active);
3441	}	4231	}
3442	}	4232	}
…		…
3444	ev_stop (EV_A_ (W)w);	4234	ev_stop (EV_A_ (W)w);
3445		4235
3446	EV_FREQUENT_CHECK;	4236	EV_FREQUENT_CHECK;
3447	}	4237	}
3448		4238
3449	void noinline	4239	ecb_noinline
		4240	void
3450	ev_periodic_again (EV_P_ ev_periodic *w) EV_THROW	4241	ev_periodic_again (EV_P_ ev_periodic *w) EV_NOEXCEPT
3451	{	4242	{
3452	/* TODO: use adjustheap and recalculation */	4243	/* TODO: use adjustheap and recalculation */
3453	ev_periodic_stop (EV_A_ w);	4244	ev_periodic_stop (EV_A_ w);
3454	ev_periodic_start (EV_A_ w);	4245	ev_periodic_start (EV_A_ w);
3455	}	4246	}
…		…
3459	# define SA_RESTART 0	4250	# define SA_RESTART 0
3460	#endif	4251	#endif
3461		4252
3462	#if EV_SIGNAL_ENABLE	4253	#if EV_SIGNAL_ENABLE
3463		4254
3464	void noinline	4255	ecb_noinline
		4256	void
3465	ev_signal_start (EV_P_ ev_signal *w) EV_THROW	4257	ev_signal_start (EV_P_ ev_signal *w) EV_NOEXCEPT
3466	{	4258	{
3467	if (expect_false (ev_is_active (w)))	4259	if (ecb_expect_false (ev_is_active (w)))
3468	return;	4260	return;
3469		4261
3470	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));	4262	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));
3471		4263
3472	#if EV_MULTIPLICITY	4264	#if EV_MULTIPLICITY
3473	assert (("libev: a signal must not be attached to two different loops",	4265	assert (("libev: a signal must not be attached to two different loops",
3474	!signals [w->signum - 1].loop || signals [w->signum - 1].loop == loop));	4266	!signals [w->signum - 1].loop || signals [w->signum - 1].loop == loop));
3475		4267
3476	signals [w->signum - 1].loop = EV_A;	4268	signals [w->signum - 1].loop = EV_A;
		4269	ECB_MEMORY_FENCE_RELEASE;
3477	#endif	4270	#endif
3478		4271
3479	EV_FREQUENT_CHECK;	4272	EV_FREQUENT_CHECK;
3480		4273
3481	#if EV_USE_SIGNALFD	4274	#if EV_USE_SIGNALFD
…		…
3540	}	4333	}
3541		4334
3542	EV_FREQUENT_CHECK;	4335	EV_FREQUENT_CHECK;
3543	}	4336	}
3544		4337
3545	void noinline	4338	ecb_noinline
		4339	void
3546	ev_signal_stop (EV_P_ ev_signal *w) EV_THROW	4340	ev_signal_stop (EV_P_ ev_signal *w) EV_NOEXCEPT
3547	{	4341	{
3548	clear_pending (EV_A_ (W)w);	4342	clear_pending (EV_A_ (W)w);
3549	if (expect_false (!ev_is_active (w)))	4343	if (ecb_expect_false (!ev_is_active (w)))
3550	return;	4344	return;
3551		4345
3552	EV_FREQUENT_CHECK;	4346	EV_FREQUENT_CHECK;
3553		4347
3554	wlist_del (&signals [w->signum - 1].head, (WL)w);	4348	wlist_del (&signals [w->signum - 1].head, (WL)w);
…		…
3582	#endif	4376	#endif
3583		4377
3584	#if EV_CHILD_ENABLE	4378	#if EV_CHILD_ENABLE
3585		4379
3586	void	4380	void
3587	ev_child_start (EV_P_ ev_child *w) EV_THROW	4381	ev_child_start (EV_P_ ev_child *w) EV_NOEXCEPT
3588	{	4382	{
3589	#if EV_MULTIPLICITY	4383	#if EV_MULTIPLICITY
3590	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));	4384	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));
3591	#endif	4385	#endif
3592	if (expect_false (ev_is_active (w)))	4386	if (ecb_expect_false (ev_is_active (w)))
3593	return;	4387	return;
3594		4388
3595	EV_FREQUENT_CHECK;	4389	EV_FREQUENT_CHECK;
3596		4390
3597	ev_start (EV_A_ (W)w, 1);	4391	ev_start (EV_A_ (W)w, 1);
…		…
3599		4393
3600	EV_FREQUENT_CHECK;	4394	EV_FREQUENT_CHECK;
3601	}	4395	}
3602		4396
3603	void	4397	void
3604	ev_child_stop (EV_P_ ev_child *w) EV_THROW	4398	ev_child_stop (EV_P_ ev_child *w) EV_NOEXCEPT
3605	{	4399	{
3606	clear_pending (EV_A_ (W)w);	4400	clear_pending (EV_A_ (W)w);
3607	if (expect_false (!ev_is_active (w)))	4401	if (ecb_expect_false (!ev_is_active (w)))
3608	return;	4402	return;
3609		4403
3610	EV_FREQUENT_CHECK;	4404	EV_FREQUENT_CHECK;
3611		4405
3612	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);	4406	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);
…		…
3626		4420
3627	#define DEF_STAT_INTERVAL 5.0074891	4421	#define DEF_STAT_INTERVAL 5.0074891
3628	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */	4422	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */
3629	#define MIN_STAT_INTERVAL 0.1074891	4423	#define MIN_STAT_INTERVAL 0.1074891
3630		4424
3631	static void noinline stat_timer_cb (EV_P_ ev_timer *w_, int revents);	4425	ecb_noinline static void stat_timer_cb (EV_P_ ev_timer *w_, int revents);
3632		4426
3633	#if EV_USE_INOTIFY	4427	#if EV_USE_INOTIFY
3634		4428
3635	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */	4429	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */
3636	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)	4430	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)
3637		4431
3638	static void noinline	4432	ecb_noinline
		4433	static void
3639	infy_add (EV_P_ ev_stat *w)	4434	infy_add (EV_P_ ev_stat *w)
3640	{	4435	{
3641	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);	4436	w->wd = inotify_add_watch (fs_fd, w->path,
		4437	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY
		4438	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO
		4439	| IN_DONT_FOLLOW | IN_MASK_ADD);
3642		4440
3643	if (w->wd >= 0)	4441	if (w->wd >= 0)
3644	{	4442	{
3645	struct statfs sfs;	4443	struct statfs sfs;
3646		4444
…		…
3650		4448
3651	if (!fs_2625)	4449	if (!fs_2625)
3652	w->timer.repeat = w->interval ? w->interval : DEF_STAT_INTERVAL;	4450	w->timer.repeat = w->interval ? w->interval : DEF_STAT_INTERVAL;
3653	else if (!statfs (w->path, &sfs)	4451	else if (!statfs (w->path, &sfs)
3654	&& (sfs.f_type == 0x1373 /* devfs */	4452	&& (sfs.f_type == 0x1373 /* devfs */
		4453	|| sfs.f_type == 0x4006 /* fat */
		4454	|| sfs.f_type == 0x4d44 /* msdos */
3655	|| sfs.f_type == 0xEF53 /* ext2/3 */	4455	|| sfs.f_type == 0xEF53 /* ext2/3 */
		4456	|| sfs.f_type == 0x72b6 /* jffs2 */
		4457	|| sfs.f_type == 0x858458f6 /* ramfs */
		4458	|| sfs.f_type == 0x5346544e /* ntfs */
3656	|| sfs.f_type == 0x3153464a /* jfs */	4459	|| sfs.f_type == 0x3153464a /* jfs */
		4460	|| sfs.f_type == 0x9123683e /* btrfs */
3657	|| sfs.f_type == 0x52654973 /* reiser3 */	4461	|| sfs.f_type == 0x52654973 /* reiser3 */
3658	|| sfs.f_type == 0x01021994 /* tempfs */	4462	|| sfs.f_type == 0x01021994 /* tmpfs */
3659	|| sfs.f_type == 0x58465342 /* xfs */))	4463	|| sfs.f_type == 0x58465342 /* xfs */))
3660	w->timer.repeat = 0.; /* filesystem is local, kernel new enough */	4464	w->timer.repeat = 0.; /* filesystem is local, kernel new enough */
3661	else	4465	else
3662	w->timer.repeat = w->interval ? w->interval : NFS_STAT_INTERVAL; /* remote, use reduced frequency */	4466	w->timer.repeat = w->interval ? w->interval : NFS_STAT_INTERVAL; /* remote, use reduced frequency */
3663	}	4467	}
…		…
3698	if (ev_is_active (&w->timer)) ev_ref (EV_A);	4502	if (ev_is_active (&w->timer)) ev_ref (EV_A);
3699	ev_timer_again (EV_A_ &w->timer);	4503	ev_timer_again (EV_A_ &w->timer);
3700	if (ev_is_active (&w->timer)) ev_unref (EV_A);	4504	if (ev_is_active (&w->timer)) ev_unref (EV_A);
3701	}	4505	}
3702		4506
3703	static void noinline	4507	ecb_noinline
		4508	static void
3704	infy_del (EV_P_ ev_stat *w)	4509	infy_del (EV_P_ ev_stat *w)
3705	{	4510	{
3706	int slot;	4511	int slot;
3707	int wd = w->wd;	4512	int wd = w->wd;
3708		4513
…		…
3715		4520
3716	/* remove this watcher, if others are watching it, they will rearm */	4521	/* remove this watcher, if others are watching it, they will rearm */
3717	inotify_rm_watch (fs_fd, wd);	4522	inotify_rm_watch (fs_fd, wd);
3718	}	4523	}
3719		4524
3720	static void noinline	4525	ecb_noinline
		4526	static void
3721	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)	4527	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)
3722	{	4528	{
3723	if (slot < 0)	4529	if (slot < 0)
3724	/* overflow, need to check for all hash slots */	4530	/* overflow, need to check for all hash slots */
3725	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)	4531	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)
…		…
3761	infy_wd (EV_A_ ev->wd, ev->wd, ev);	4567	infy_wd (EV_A_ ev->wd, ev->wd, ev);
3762	ofs += sizeof (struct inotify_event) + ev->len;	4568	ofs += sizeof (struct inotify_event) + ev->len;
3763	}	4569	}
3764	}	4570	}
3765		4571
3766	inline_size void ecb_cold	4572	inline_size ecb_cold
		4573	void
3767	ev_check_2625 (EV_P)	4574	ev_check_2625 (EV_P)
3768	{	4575	{
3769	/* kernels < 2.6.25 are borked	4576	/* kernels < 2.6.25 are borked
3770	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html	4577	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html
3771	*/	4578	*/
…		…
3861	#else	4668	#else
3862	# define EV_LSTAT(p,b) lstat (p, b)	4669	# define EV_LSTAT(p,b) lstat (p, b)
3863	#endif	4670	#endif
3864		4671
3865	void	4672	void
3866	ev_stat_stat (EV_P_ ev_stat *w) EV_THROW	4673	ev_stat_stat (EV_P_ ev_stat *w) EV_NOEXCEPT
3867	{	4674	{
3868	if (lstat (w->path, &w->attr) < 0)	4675	if (lstat (w->path, &w->attr) < 0)
3869	w->attr.st_nlink = 0;	4676	w->attr.st_nlink = 0;
3870	else if (!w->attr.st_nlink)	4677	else if (!w->attr.st_nlink)
3871	w->attr.st_nlink = 1;	4678	w->attr.st_nlink = 1;
3872	}	4679	}
3873		4680
3874	static void noinline	4681	ecb_noinline
		4682	static void
3875	stat_timer_cb (EV_P_ ev_timer *w_, int revents)	4683	stat_timer_cb (EV_P_ ev_timer *w_, int revents)
3876	{	4684	{
3877	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));	4685	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));
3878		4686
3879	ev_statdata prev = w->attr;	4687	ev_statdata prev = w->attr;
…		…
3910	ev_feed_event (EV_A_ w, EV_STAT);	4718	ev_feed_event (EV_A_ w, EV_STAT);
3911	}	4719	}
3912	}	4720	}
3913		4721
3914	void	4722	void
3915	ev_stat_start (EV_P_ ev_stat *w) EV_THROW	4723	ev_stat_start (EV_P_ ev_stat *w) EV_NOEXCEPT
3916	{	4724	{
3917	if (expect_false (ev_is_active (w)))	4725	if (ecb_expect_false (ev_is_active (w)))
3918	return;	4726	return;
3919		4727
3920	ev_stat_stat (EV_A_ w);	4728	ev_stat_stat (EV_A_ w);
3921		4729
3922	if (w->interval < MIN_STAT_INTERVAL && w->interval)	4730	if (w->interval < MIN_STAT_INTERVAL && w->interval)
…		…
3941		4749
3942	EV_FREQUENT_CHECK;	4750	EV_FREQUENT_CHECK;
3943	}	4751	}
3944		4752
3945	void	4753	void
3946	ev_stat_stop (EV_P_ ev_stat *w) EV_THROW	4754	ev_stat_stop (EV_P_ ev_stat *w) EV_NOEXCEPT
3947	{	4755	{
3948	clear_pending (EV_A_ (W)w);	4756	clear_pending (EV_A_ (W)w);
3949	if (expect_false (!ev_is_active (w)))	4757	if (ecb_expect_false (!ev_is_active (w)))
3950	return;	4758	return;
3951		4759
3952	EV_FREQUENT_CHECK;	4760	EV_FREQUENT_CHECK;
3953		4761
3954	#if EV_USE_INOTIFY	4762	#if EV_USE_INOTIFY
…		…
3967	}	4775	}
3968	#endif	4776	#endif
3969		4777
3970	#if EV_IDLE_ENABLE	4778	#if EV_IDLE_ENABLE
3971	void	4779	void
3972	ev_idle_start (EV_P_ ev_idle *w) EV_THROW	4780	ev_idle_start (EV_P_ ev_idle *w) EV_NOEXCEPT
3973	{	4781	{
3974	if (expect_false (ev_is_active (w)))	4782	if (ecb_expect_false (ev_is_active (w)))
3975	return;	4783	return;
3976		4784
3977	pri_adjust (EV_A_ (W)w);	4785	pri_adjust (EV_A_ (W)w);
3978		4786
3979	EV_FREQUENT_CHECK;	4787	EV_FREQUENT_CHECK;
…		…
3982	int active = ++idlecnt [ABSPRI (w)];	4790	int active = ++idlecnt [ABSPRI (w)];
3983		4791
3984	++idleall;	4792	++idleall;
3985	ev_start (EV_A_ (W)w, active);	4793	ev_start (EV_A_ (W)w, active);
3986		4794
3987	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, EMPTY2);	4795	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, array_needsize_noinit);
3988	idles [ABSPRI (w)][active - 1] = w;	4796	idles [ABSPRI (w)][active - 1] = w;
3989	}	4797	}
3990		4798
3991	EV_FREQUENT_CHECK;	4799	EV_FREQUENT_CHECK;
3992	}	4800	}
3993		4801
3994	void	4802	void
3995	ev_idle_stop (EV_P_ ev_idle *w) EV_THROW	4803	ev_idle_stop (EV_P_ ev_idle *w) EV_NOEXCEPT
3996	{	4804	{
3997	clear_pending (EV_A_ (W)w);	4805	clear_pending (EV_A_ (W)w);
3998	if (expect_false (!ev_is_active (w)))	4806	if (ecb_expect_false (!ev_is_active (w)))
3999	return;	4807	return;
4000		4808
4001	EV_FREQUENT_CHECK;	4809	EV_FREQUENT_CHECK;
4002		4810
4003	{	4811	{
…		…
4014	}	4822	}
4015	#endif	4823	#endif
4016		4824
4017	#if EV_PREPARE_ENABLE	4825	#if EV_PREPARE_ENABLE
4018	void	4826	void
4019	ev_prepare_start (EV_P_ ev_prepare *w) EV_THROW	4827	ev_prepare_start (EV_P_ ev_prepare *w) EV_NOEXCEPT
4020	{	4828	{
4021	if (expect_false (ev_is_active (w)))	4829	if (ecb_expect_false (ev_is_active (w)))
4022	return;	4830	return;
4023		4831
4024	EV_FREQUENT_CHECK;	4832	EV_FREQUENT_CHECK;
4025		4833
4026	ev_start (EV_A_ (W)w, ++preparecnt);	4834	ev_start (EV_A_ (W)w, ++preparecnt);
4027	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, EMPTY2);	4835	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, array_needsize_noinit);
4028	prepares [preparecnt - 1] = w;	4836	prepares [preparecnt - 1] = w;
4029		4837
4030	EV_FREQUENT_CHECK;	4838	EV_FREQUENT_CHECK;
4031	}	4839	}
4032		4840
4033	void	4841	void
4034	ev_prepare_stop (EV_P_ ev_prepare *w) EV_THROW	4842	ev_prepare_stop (EV_P_ ev_prepare *w) EV_NOEXCEPT
4035	{	4843	{
4036	clear_pending (EV_A_ (W)w);	4844	clear_pending (EV_A_ (W)w);
4037	if (expect_false (!ev_is_active (w)))	4845	if (ecb_expect_false (!ev_is_active (w)))
4038	return;	4846	return;
4039		4847
4040	EV_FREQUENT_CHECK;	4848	EV_FREQUENT_CHECK;
4041		4849
4042	{	4850	{
…		…
4052	}	4860	}
4053	#endif	4861	#endif
4054		4862
4055	#if EV_CHECK_ENABLE	4863	#if EV_CHECK_ENABLE
4056	void	4864	void
4057	ev_check_start (EV_P_ ev_check *w) EV_THROW	4865	ev_check_start (EV_P_ ev_check *w) EV_NOEXCEPT
4058	{	4866	{
4059	if (expect_false (ev_is_active (w)))	4867	if (ecb_expect_false (ev_is_active (w)))
4060	return;	4868	return;
4061		4869
4062	EV_FREQUENT_CHECK;	4870	EV_FREQUENT_CHECK;
4063		4871
4064	ev_start (EV_A_ (W)w, ++checkcnt);	4872	ev_start (EV_A_ (W)w, ++checkcnt);
4065	array_needsize (ev_check *, checks, checkmax, checkcnt, EMPTY2);	4873	array_needsize (ev_check *, checks, checkmax, checkcnt, array_needsize_noinit);
4066	checks [checkcnt - 1] = w;	4874	checks [checkcnt - 1] = w;
4067		4875
4068	EV_FREQUENT_CHECK;	4876	EV_FREQUENT_CHECK;
4069	}	4877	}
4070		4878
4071	void	4879	void
4072	ev_check_stop (EV_P_ ev_check *w) EV_THROW	4880	ev_check_stop (EV_P_ ev_check *w) EV_NOEXCEPT
4073	{	4881	{
4074	clear_pending (EV_A_ (W)w);	4882	clear_pending (EV_A_ (W)w);
4075	if (expect_false (!ev_is_active (w)))	4883	if (ecb_expect_false (!ev_is_active (w)))
4076	return;	4884	return;
4077		4885
4078	EV_FREQUENT_CHECK;	4886	EV_FREQUENT_CHECK;
4079		4887
4080	{	4888	{
…		…
4089	EV_FREQUENT_CHECK;	4897	EV_FREQUENT_CHECK;
4090	}	4898	}
4091	#endif	4899	#endif
4092		4900
4093	#if EV_EMBED_ENABLE	4901	#if EV_EMBED_ENABLE
4094	void noinline	4902	ecb_noinline
		4903	void
4095	ev_embed_sweep (EV_P_ ev_embed *w) EV_THROW	4904	ev_embed_sweep (EV_P_ ev_embed *w) EV_NOEXCEPT
4096	{	4905	{
4097	ev_run (w->other, EVRUN_NOWAIT);	4906	ev_run (w->other, EVRUN_NOWAIT);
4098	}	4907	}
4099		4908
4100	static void	4909	static void
…		…
4148	ev_idle_stop (EV_A_ idle);	4957	ev_idle_stop (EV_A_ idle);
4149	}	4958	}
4150	#endif	4959	#endif
4151		4960
4152	void	4961	void
4153	ev_embed_start (EV_P_ ev_embed *w) EV_THROW	4962	ev_embed_start (EV_P_ ev_embed *w) EV_NOEXCEPT
4154	{	4963	{
4155	if (expect_false (ev_is_active (w)))	4964	if (ecb_expect_false (ev_is_active (w)))
4156	return;	4965	return;
4157		4966
4158	{	4967	{
4159	EV_P = w->other;	4968	EV_P = w->other;
4160	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));	4969	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));
…		…
4179		4988
4180	EV_FREQUENT_CHECK;	4989	EV_FREQUENT_CHECK;
4181	}	4990	}
4182		4991
4183	void	4992	void
4184	ev_embed_stop (EV_P_ ev_embed *w) EV_THROW	4993	ev_embed_stop (EV_P_ ev_embed *w) EV_NOEXCEPT
4185	{	4994	{
4186	clear_pending (EV_A_ (W)w);	4995	clear_pending (EV_A_ (W)w);
4187	if (expect_false (!ev_is_active (w)))	4996	if (ecb_expect_false (!ev_is_active (w)))
4188	return;	4997	return;
4189		4998
4190	EV_FREQUENT_CHECK;	4999	EV_FREQUENT_CHECK;
4191		5000
4192	ev_io_stop (EV_A_ &w->io);	5001	ev_io_stop (EV_A_ &w->io);
…		…
4199	}	5008	}
4200	#endif	5009	#endif
4201		5010
4202	#if EV_FORK_ENABLE	5011	#if EV_FORK_ENABLE
4203	void	5012	void
4204	ev_fork_start (EV_P_ ev_fork *w) EV_THROW	5013	ev_fork_start (EV_P_ ev_fork *w) EV_NOEXCEPT
4205	{	5014	{
4206	if (expect_false (ev_is_active (w)))	5015	if (ecb_expect_false (ev_is_active (w)))
4207	return;	5016	return;
4208		5017
4209	EV_FREQUENT_CHECK;	5018	EV_FREQUENT_CHECK;
4210		5019
4211	ev_start (EV_A_ (W)w, ++forkcnt);	5020	ev_start (EV_A_ (W)w, ++forkcnt);
4212	array_needsize (ev_fork *, forks, forkmax, forkcnt, EMPTY2);	5021	array_needsize (ev_fork *, forks, forkmax, forkcnt, array_needsize_noinit);
4213	forks [forkcnt - 1] = w;	5022	forks [forkcnt - 1] = w;
4214		5023
4215	EV_FREQUENT_CHECK;	5024	EV_FREQUENT_CHECK;
4216	}	5025	}
4217		5026
4218	void	5027	void
4219	ev_fork_stop (EV_P_ ev_fork *w) EV_THROW	5028	ev_fork_stop (EV_P_ ev_fork *w) EV_NOEXCEPT
4220	{	5029	{
4221	clear_pending (EV_A_ (W)w);	5030	clear_pending (EV_A_ (W)w);
4222	if (expect_false (!ev_is_active (w)))	5031	if (ecb_expect_false (!ev_is_active (w)))
4223	return;	5032	return;
4224		5033
4225	EV_FREQUENT_CHECK;	5034	EV_FREQUENT_CHECK;
4226		5035
4227	{	5036	{
…		…
4237	}	5046	}
4238	#endif	5047	#endif
4239		5048
4240	#if EV_CLEANUP_ENABLE	5049	#if EV_CLEANUP_ENABLE
4241	void	5050	void
4242	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_THROW	5051	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4243	{	5052	{
4244	if (expect_false (ev_is_active (w)))	5053	if (ecb_expect_false (ev_is_active (w)))
4245	return;	5054	return;
4246		5055
4247	EV_FREQUENT_CHECK;	5056	EV_FREQUENT_CHECK;
4248		5057
4249	ev_start (EV_A_ (W)w, ++cleanupcnt);	5058	ev_start (EV_A_ (W)w, ++cleanupcnt);
4250	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, EMPTY2);	5059	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, array_needsize_noinit);
4251	cleanups [cleanupcnt - 1] = w;	5060	cleanups [cleanupcnt - 1] = w;
4252		5061
4253	/* cleanup watchers should never keep a refcount on the loop */	5062	/* cleanup watchers should never keep a refcount on the loop */
4254	ev_unref (EV_A);	5063	ev_unref (EV_A);
4255	EV_FREQUENT_CHECK;	5064	EV_FREQUENT_CHECK;
4256	}	5065	}
4257		5066
4258	void	5067	void
4259	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_THROW	5068	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4260	{	5069	{
4261	clear_pending (EV_A_ (W)w);	5070	clear_pending (EV_A_ (W)w);
4262	if (expect_false (!ev_is_active (w)))	5071	if (ecb_expect_false (!ev_is_active (w)))
4263	return;	5072	return;
4264		5073
4265	EV_FREQUENT_CHECK;	5074	EV_FREQUENT_CHECK;
4266	ev_ref (EV_A);	5075	ev_ref (EV_A);
4267		5076
…		…
4278	}	5087	}
4279	#endif	5088	#endif
4280		5089
4281	#if EV_ASYNC_ENABLE	5090	#if EV_ASYNC_ENABLE
4282	void	5091	void
4283	ev_async_start (EV_P_ ev_async *w) EV_THROW	5092	ev_async_start (EV_P_ ev_async *w) EV_NOEXCEPT
4284	{	5093	{
4285	if (expect_false (ev_is_active (w)))	5094	if (ecb_expect_false (ev_is_active (w)))
4286	return;	5095	return;
4287		5096
4288	w->sent = 0;	5097	w->sent = 0;
4289		5098
4290	evpipe_init (EV_A);	5099	evpipe_init (EV_A);
4291		5100
4292	EV_FREQUENT_CHECK;	5101	EV_FREQUENT_CHECK;
4293		5102
4294	ev_start (EV_A_ (W)w, ++asynccnt);	5103	ev_start (EV_A_ (W)w, ++asynccnt);
4295	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, EMPTY2);	5104	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, array_needsize_noinit);
4296	asyncs [asynccnt - 1] = w;	5105	asyncs [asynccnt - 1] = w;
4297		5106
4298	EV_FREQUENT_CHECK;	5107	EV_FREQUENT_CHECK;
4299	}	5108	}
4300		5109
4301	void	5110	void
4302	ev_async_stop (EV_P_ ev_async *w) EV_THROW	5111	ev_async_stop (EV_P_ ev_async *w) EV_NOEXCEPT
4303	{	5112	{
4304	clear_pending (EV_A_ (W)w);	5113	clear_pending (EV_A_ (W)w);
4305	if (expect_false (!ev_is_active (w)))	5114	if (ecb_expect_false (!ev_is_active (w)))
4306	return;	5115	return;
4307		5116
4308	EV_FREQUENT_CHECK;	5117	EV_FREQUENT_CHECK;
4309		5118
4310	{	5119	{
…		…
4318		5127
4319	EV_FREQUENT_CHECK;	5128	EV_FREQUENT_CHECK;
4320	}	5129	}
4321		5130
4322	void	5131	void
4323	ev_async_send (EV_P_ ev_async *w) EV_THROW	5132	ev_async_send (EV_P_ ev_async *w) EV_NOEXCEPT
4324	{	5133	{
4325	w->sent = 1;	5134	w->sent = 1;
4326	evpipe_write (EV_A_ &async_pending);	5135	evpipe_write (EV_A_ &async_pending);
4327	}	5136	}
4328	#endif	5137	#endif
…		…
4365		5174
4366	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));	5175	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));
4367	}	5176	}
4368		5177
4369	void	5178	void
4370	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_THROW	5179	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_NOEXCEPT
4371	{	5180	{
4372	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));	5181	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));
4373
4374	if (expect_false (!once))
4375	{
4376	cb (EV_ERROR | EV_READ | EV_WRITE | EV_TIMER, arg);
4377	return;
4378	}
4379		5182
4380	once->cb = cb;	5183	once->cb = cb;
4381	once->arg = arg;	5184	once->arg = arg;
4382		5185
4383	ev_init (&once->io, once_cb_io);	5186	ev_init (&once->io, once_cb_io);
…		…
4396	}	5199	}
4397		5200
4398	/*****************************************************************************/	5201	/*****************************************************************************/
4399		5202
4400	#if EV_WALK_ENABLE	5203	#if EV_WALK_ENABLE
4401	void ecb_cold	5204	ecb_cold
		5205	void
4402	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_THROW	5206	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_NOEXCEPT
4403	{	5207	{
4404	int i, j;	5208	int i, j;
4405	ev_watcher_list *wl, *wn;	5209	ev_watcher_list *wl, *wn;
4406		5210
4407	if (types & (EV_IO | EV_EMBED))	5211	if (types & (EV_IO | EV_EMBED))

Diff Legend

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