ViewVC Help

View File | Revision Log | Show Annotations | Download File

/cvs/libev/ev.c

Comparing libev/ev.c (file contents):
Revision 1.436 by root, Tue May 29 20:44:39 2012 UTC vs.
Revision 1.501 by root, Mon Jul 1 21:47:42 2019 UTC

1	/*	1	/*
2	* libev event processing core, watcher management	2	* libev event processing core, watcher management
3	*	3	*
4	* Copyright (c) 2007,2008,2009,2010,2011,2012 Marc Alexander Lehmann <libev@schmorp.de>	4	* Copyright (c) 2007-2019 Marc Alexander Lehmann <libev@schmorp.de>
5	* All rights reserved.	5	* All rights reserved.
6	*	6	*
7	* Redistribution and use in source and binary forms, with or without modifica-	7	* Redistribution and use in source and binary forms, with or without modifica-
8	* tion, are permitted provided that the following conditions are met:	8	* tion, are permitted provided that the following conditions are met:
9	*	9	*
…		…
43	# include EV_CONFIG_H	43	# include EV_CONFIG_H
44	# else	44	# else
45	# include "config.h"	45	# include "config.h"
46	# endif	46	# endif
47		47
48	#if HAVE_FLOOR	48	# if HAVE_FLOOR
49	# ifndef EV_USE_FLOOR	49	# ifndef EV_USE_FLOOR
50	# define EV_USE_FLOOR 1	50	# define EV_USE_FLOOR 1
		51	# endif
51	# endif	52	# endif
52	#endif
53		53
54	# if HAVE_CLOCK_SYSCALL	54	# if HAVE_CLOCK_SYSCALL
55	# ifndef EV_USE_CLOCK_SYSCALL	55	# ifndef EV_USE_CLOCK_SYSCALL
56	# define EV_USE_CLOCK_SYSCALL 1	56	# define EV_USE_CLOCK_SYSCALL 1
57	# ifndef EV_USE_REALTIME	57	# ifndef EV_USE_REALTIME
…		…
113	# define EV_USE_EPOLL EV_FEATURE_BACKENDS	113	# define EV_USE_EPOLL EV_FEATURE_BACKENDS
114	# endif	114	# endif
115	# else	115	# else
116	# undef EV_USE_EPOLL	116	# undef EV_USE_EPOLL
117	# define EV_USE_EPOLL 0	117	# define EV_USE_EPOLL 0
		118	# endif
		119
		120	# if HAVE_LINUX_AIO_ABI_H
		121	# ifndef EV_USE_LINUXAIO
		122	# define EV_USE_LINUXAIO EV_FEATURE_BACKENDS
		123	# endif
		124	# else
		125	# undef EV_USE_LINUXAIO
		126	# define EV_USE_LINUXAIO 0
118	# endif	127	# endif
119		128
120	# if HAVE_KQUEUE && HAVE_SYS_EVENT_H	129	# if HAVE_KQUEUE && HAVE_SYS_EVENT_H
121	# ifndef EV_USE_KQUEUE	130	# ifndef EV_USE_KQUEUE
122	# define EV_USE_KQUEUE EV_FEATURE_BACKENDS	131	# define EV_USE_KQUEUE EV_FEATURE_BACKENDS
…		…
162	# define EV_USE_EVENTFD 0	171	# define EV_USE_EVENTFD 0
163	# endif	172	# endif
164		173
165	#endif	174	#endif
166		175
		176	/* OS X, in its infinite idiocy, actually HARDCODES
		177	* a limit of 1024 into their select. Where people have brains,
		178	* OS X engineers apparently have a vacuum. Or maybe they were
		179	* ordered to have a vacuum, or they do anything for money.
		180	* This might help. Or not.
		181	* Note that this must be defined early, as other include files
		182	* will rely on this define as well.
		183	*/
		184	#define _DARWIN_UNLIMITED_SELECT 1
		185
167	#include <stdlib.h>	186	#include <stdlib.h>
168	#include <string.h>	187	#include <string.h>
169	#include <fcntl.h>	188	#include <fcntl.h>
170	#include <stddef.h>	189	#include <stddef.h>
171		190
…		…
208	# ifndef EV_SELECT_IS_WINSOCKET	227	# ifndef EV_SELECT_IS_WINSOCKET
209	# define EV_SELECT_IS_WINSOCKET 1	228	# define EV_SELECT_IS_WINSOCKET 1
210	# endif	229	# endif
211	# undef EV_AVOID_STDIO	230	# undef EV_AVOID_STDIO
212	#endif	231	#endif
213
214	/* OS X, in its infinite idiocy, actually HARDCODES
215	* a limit of 1024 into their select. Where people have brains,
216	* OS X engineers apparently have a vacuum. Or maybe they were
217	* ordered to have a vacuum, or they do anything for money.
218	* This might help. Or not.
219	*/
220	#define _DARWIN_UNLIMITED_SELECT 1
221		232
222	/* this block tries to deduce configuration from header-defined symbols and defaults */	233	/* this block tries to deduce configuration from header-defined symbols and defaults */
223		234
224	/* try to deduce the maximum number of signals on this platform */	235	/* try to deduce the maximum number of signals on this platform */
225	#if defined EV_NSIG	236	#if defined EV_NSIG
…		…
241	#elif defined SIGARRAYSIZE	252	#elif defined SIGARRAYSIZE
242	# define EV_NSIG (SIGARRAYSIZE) /* Assume ary[SIGARRAYSIZE] */	253	# define EV_NSIG (SIGARRAYSIZE) /* Assume ary[SIGARRAYSIZE] */
243	#elif defined _sys_nsig	254	#elif defined _sys_nsig
244	# define EV_NSIG (_sys_nsig) /* Solaris 2.5 */	255	# define EV_NSIG (_sys_nsig) /* Solaris 2.5 */
245	#else	256	#else
246	# error "unable to find value for NSIG, please report"	257	# define EV_NSIG (8 * sizeof (sigset_t) + 1)
247	/* to make it compile regardless, just remove the above line, */
248	/* but consider reporting it, too! :) */
249	# define EV_NSIG 65
250	#endif	258	#endif
251		259
252	#ifndef EV_USE_FLOOR	260	#ifndef EV_USE_FLOOR
253	# define EV_USE_FLOOR 0	261	# define EV_USE_FLOOR 0
254	#endif	262	#endif
255		263
256	#ifndef EV_USE_CLOCK_SYSCALL	264	#ifndef EV_USE_CLOCK_SYSCALL
257	# if __linux && __GLIBC__ >= 2	265	# if __linux && __GLIBC__ == 2 && __GLIBC_MINOR__ < 17
258	# define EV_USE_CLOCK_SYSCALL EV_FEATURE_OS	266	# define EV_USE_CLOCK_SYSCALL EV_FEATURE_OS
259	# else	267	# else
260	# define EV_USE_CLOCK_SYSCALL 0	268	# define EV_USE_CLOCK_SYSCALL 0
		269	# endif
		270	#endif
		271
		272	#if !(_POSIX_TIMERS > 0)
		273	# ifndef EV_USE_MONOTONIC
		274	# define EV_USE_MONOTONIC 0
		275	# endif
		276	# ifndef EV_USE_REALTIME
		277	# define EV_USE_REALTIME 0
261	# endif	278	# endif
262	#endif	279	#endif
263		280
264	#ifndef EV_USE_MONOTONIC	281	#ifndef EV_USE_MONOTONIC
265	# if defined _POSIX_MONOTONIC_CLOCK && _POSIX_MONOTONIC_CLOCK >= 0	282	# if defined _POSIX_MONOTONIC_CLOCK && _POSIX_MONOTONIC_CLOCK >= 0
…		…
307		324
308	#ifndef EV_USE_PORT	325	#ifndef EV_USE_PORT
309	# define EV_USE_PORT 0	326	# define EV_USE_PORT 0
310	#endif	327	#endif
311		328
		329	#ifndef EV_USE_LINUXAIO
		330	# if __linux /* libev currently assumes linux/aio_abi.h is always available on linux */
		331	# define EV_USE_LINUXAIO 1
		332	# else
		333	# define EV_USE_LINUXAIO 0
		334	# endif
		335	#endif
		336
		337	#ifndef EV_USE_IOURING
		338	# if __linux
		339	# define EV_USE_IOURING 0
		340	# else
		341	# define EV_USE_IOURING 0
		342	# endif
		343	#endif
		344
312	#ifndef EV_USE_INOTIFY	345	#ifndef EV_USE_INOTIFY
313	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))	346	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))
314	# define EV_USE_INOTIFY EV_FEATURE_OS	347	# define EV_USE_INOTIFY EV_FEATURE_OS
315	# else	348	# else
316	# define EV_USE_INOTIFY 0	349	# define EV_USE_INOTIFY 0
…		…
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 /* ev_linxaio uses ev_poll.c:ev_epoll_create */
		453	# undef EV_USE_LINUXAIO
		454	# define EV_USE_LINUXAIO 0
		455	# else
		456	# define EV_NEED_SYSCALL 1
		457	# endif
		458	#endif
		459
		460	#if EV_USE_IOURING
		461	# include <sys/syscall.h>
		462	# if !__alpha && !SYS_io_uring_setup
		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
		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>
…		…
449	uint32_t ssi_signo;	518	uint32_t ssi_signo;
450	char pad[128 - sizeof (uint32_t)];	519	char pad[128 - sizeof (uint32_t)];
451	};	520	};
452	#endif	521	#endif
453		522
454	/**/	523	/*****************************************************************************/
		524
		525	#if EV_NEED_SYSCALL
		526
		527	#include <sys/syscall.h>
		528
		529	/*
		530	* define some syscall wrappers for common architectures
		531	* this is mostly for nice looks during debugging, not performance.
		532	* our syscalls return < 0, not == -1, on error. which is good
		533	* enough for linux aio.
		534	* TODO: arm is also common nowadays, maybe even mips and x86
		535	* TODO: after implementing this, it suddenly looks like overkill, but its hard to remove...
		536	*/
		537	#if __GNUC__ && __linux && ECB_AMD64 && !defined __OPTIMIZE_SIZE__
		538	/* the costly errno access probably kills this for size optimisation */
		539
		540	#define ev_syscall(nr,narg,arg1,arg2,arg3,arg4,arg5) \
		541	({ \
		542	long res; \
		543	register unsigned long r5 __asm__ ("r8" ); \
		544	register unsigned long r4 __asm__ ("r10"); \
		545	register unsigned long r3 __asm__ ("rdx"); \
		546	register unsigned long r2 __asm__ ("rsi"); \
		547	register unsigned long r1 __asm__ ("rdi"); \
		548	if (narg >= 5) r5 = (unsigned long)(arg5); \
		549	if (narg >= 4) r4 = (unsigned long)(arg4); \
		550	if (narg >= 3) r3 = (unsigned long)(arg3); \
		551	if (narg >= 2) r2 = (unsigned long)(arg2); \
		552	if (narg >= 1) r1 = (unsigned long)(arg1); \
		553	__asm__ __volatile__ ( \
		554	"syscall\n\t" \
		555	: "=a" (res) \
		556	: "0" (nr), "r" (r1), "r" (r2), "r" (r3), "r" (r4), "r" (r5) \
		557	: "cc", "r11", "cx", "memory"); \
		558	errno = -res; \
		559	res; \
		560	})
		561
		562	#endif
		563
		564	#ifdef ev_syscall
		565	#define ev_syscall0(nr) ev_syscall (nr, 0, 0, 0, 0, 0, 0
		566	#define ev_syscall1(nr,arg1) ev_syscall (nr, 1, arg1, 0, 0, 0, 0)
		567	#define ev_syscall2(nr,arg1,arg2) ev_syscall (nr, 2, arg1, arg2, 0, 0, 0)
		568	#define ev_syscall3(nr,arg1,arg2,arg3) ev_syscall (nr, 3, arg1, arg2, arg3, 0, 0)
		569	#define ev_syscall4(nr,arg1,arg2,arg3,arg4) ev_syscall (nr, 3, arg1, arg2, arg3, arg4, 0)
		570	#define ev_syscall5(nr,arg1,arg2,arg3,arg4,arg5) ev_syscall (nr, 5, arg1, arg2, arg3, arg4, arg5)
		571	#else
		572	#define ev_syscall0(nr) syscall (nr)
		573	#define ev_syscall1(nr,arg1) syscall (nr, arg1)
		574	#define ev_syscall2(nr,arg1,arg2) syscall (nr, arg1, arg2)
		575	#define ev_syscall3(nr,arg1,arg2,arg3) syscall (nr, arg1, arg2, arg3)
		576	#define ev_syscall4(nr,arg1,arg2,arg3,arg4) syscall (nr, arg1, arg2, arg3, arg4)
		577	#define ev_syscall5(nr,arg1,arg2,arg3,arg4,arg5) syscall (nr, arg1, arg2, arg3, arg4, arg5)
		578	#endif
		579
		580	#endif
		581
		582	/*****************************************************************************/
455		583
456	#if EV_VERIFY >= 3	584	#if EV_VERIFY >= 3
457	# define EV_FREQUENT_CHECK ev_verify (EV_A)	585	# define EV_FREQUENT_CHECK ev_verify (EV_A)
458	#else	586	#else
459	# define EV_FREQUENT_CHECK do { } while (0)	587	# define EV_FREQUENT_CHECK do { } while (0)
…		…
475	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */	603	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */
476	/* ECB.H BEGIN */	604	/* ECB.H BEGIN */
477	/*	605	/*
478	* libecb - http://software.schmorp.de/pkg/libecb	606	* libecb - http://software.schmorp.de/pkg/libecb
479	*	607	*
480	* Copyright (©) 2009-2012 Marc Alexander Lehmann <libecb@schmorp.de>	608	* Copyright (©) 2009-2015 Marc Alexander Lehmann <libecb@schmorp.de>
481	* Copyright (©) 2011 Emanuele Giaquinta	609	* Copyright (©) 2011 Emanuele Giaquinta
482	* All rights reserved.	610	* All rights reserved.
483	*	611	*
484	* Redistribution and use in source and binary forms, with or without modifica-	612	* Redistribution and use in source and binary forms, with or without modifica-
485	* tion, are permitted provided that the following conditions are met:	613	* tion, are permitted provided that the following conditions are met:
…		…
499	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;	627	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;
500	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,	628	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,
501	* WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING NEGLIGENCE OR OTH-	629	* WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING NEGLIGENCE OR OTH-
502	* ERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED	630	* ERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED
503	* OF THE POSSIBILITY OF SUCH DAMAGE.	631	* OF THE POSSIBILITY OF SUCH DAMAGE.
		632	*
		633	* Alternatively, the contents of this file may be used under the terms of
		634	* the GNU General Public License ("GPL") version 2 or any later version,
		635	* in which case the provisions of the GPL are applicable instead of
		636	* the above. If you wish to allow the use of your version of this file
		637	* only under the terms of the GPL and not to allow others to use your
		638	* version of this file under the BSD license, indicate your decision
		639	* by deleting the provisions above and replace them with the notice
		640	* and other provisions required by the GPL. If you do not delete the
		641	* provisions above, a recipient may use your version of this file under
		642	* either the BSD or the GPL.
504	*/	643	*/
505		644
506	#ifndef ECB_H	645	#ifndef ECB_H
507	#define ECB_H	646	#define ECB_H
		647
		648	/* 16 bits major, 16 bits minor */
		649	#define ECB_VERSION 0x00010006
508		650
509	#ifdef _WIN32	651	#ifdef _WIN32
510	typedef signed char int8_t;	652	typedef signed char int8_t;
511	typedef unsigned char uint8_t;	653	typedef unsigned char uint8_t;
512	typedef signed short int16_t;	654	typedef signed short int16_t;
…		…
518	typedef unsigned long long uint64_t;	660	typedef unsigned long long uint64_t;
519	#else /* _MSC_VER || __BORLANDC__ */	661	#else /* _MSC_VER || __BORLANDC__ */
520	typedef signed __int64 int64_t;	662	typedef signed __int64 int64_t;
521	typedef unsigned __int64 uint64_t;	663	typedef unsigned __int64 uint64_t;
522	#endif	664	#endif
		665	#ifdef _WIN64
		666	#define ECB_PTRSIZE 8
		667	typedef uint64_t uintptr_t;
		668	typedef int64_t intptr_t;
		669	#else
		670	#define ECB_PTRSIZE 4
		671	typedef uint32_t uintptr_t;
		672	typedef int32_t intptr_t;
		673	#endif
523	#else	674	#else
524	#include <inttypes.h>	675	#include <inttypes.h>
		676	#if (defined INTPTR_MAX ? INTPTR_MAX : ULONG_MAX) > 0xffffffffU
		677	#define ECB_PTRSIZE 8
		678	#else
		679	#define ECB_PTRSIZE 4
		680	#endif
		681	#endif
		682
		683	#define ECB_GCC_AMD64 (__amd64 || __amd64__ || __x86_64 || __x86_64__)
		684	#define ECB_MSVC_AMD64 (_M_AMD64 || _M_X64)
		685
		686	/* work around x32 idiocy by defining proper macros */
		687	#if ECB_GCC_AMD64 || ECB_MSVC_AMD64
		688	#if _ILP32
		689	#define ECB_AMD64_X32 1
		690	#else
		691	#define ECB_AMD64 1
		692	#endif
525	#endif	693	#endif
526		694
527	/* many compilers define _GNUC_ to some versions but then only implement	695	/* many compilers define _GNUC_ to some versions but then only implement
528	* what their idiot authors think are the "more important" extensions,	696	* what their idiot authors think are the "more important" extensions,
529	* causing enormous grief in return for some better fake benchmark numbers.	697	* causing enormous grief in return for some better fake benchmark numbers.
530	* or so.	698	* or so.
531	* we try to detect these and simply assume they are not gcc - if they have	699	* we try to detect these and simply assume they are not gcc - if they have
532	* an issue with that they should have done it right in the first place.	700	* an issue with that they should have done it right in the first place.
533	*/	701	*/
534	#ifndef ECB_GCC_VERSION
535	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__	702	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__
536	#define ECB_GCC_VERSION(major,minor) 0	703	#define ECB_GCC_VERSION(major,minor) 0
537	#else	704	#else
538	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))	705	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))
539	#endif	706	#endif
		707
		708	#define ECB_CLANG_VERSION(major,minor) (__clang_major__ > (major) || (__clang_major__ == (major) && __clang_minor__ >= (minor)))
		709
		710	#if __clang__ && defined __has_builtin
		711	#define ECB_CLANG_BUILTIN(x) __has_builtin (x)
		712	#else
		713	#define ECB_CLANG_BUILTIN(x) 0
		714	#endif
		715
		716	#if __clang__ && defined __has_extension
		717	#define ECB_CLANG_EXTENSION(x) __has_extension (x)
		718	#else
		719	#define ECB_CLANG_EXTENSION(x) 0
		720	#endif
		721
		722	#define ECB_CPP (__cplusplus+0)
		723	#define ECB_CPP11 (__cplusplus >= 201103L)
		724	#define ECB_CPP14 (__cplusplus >= 201402L)
		725	#define ECB_CPP17 (__cplusplus >= 201703L)
		726
		727	#if ECB_CPP
		728	#define ECB_C 0
		729	#define ECB_STDC_VERSION 0
		730	#else
		731	#define ECB_C 1
		732	#define ECB_STDC_VERSION __STDC_VERSION__
		733	#endif
		734
		735	#define ECB_C99 (ECB_STDC_VERSION >= 199901L)
		736	#define ECB_C11 (ECB_STDC_VERSION >= 201112L)
		737	#define ECB_C17 (ECB_STDC_VERSION >= 201710L)
		738
		739	#if ECB_CPP
		740	#define ECB_EXTERN_C extern "C"
		741	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {
		742	#define ECB_EXTERN_C_END }
		743	#else
		744	#define ECB_EXTERN_C extern
		745	#define ECB_EXTERN_C_BEG
		746	#define ECB_EXTERN_C_END
540	#endif	747	#endif
541		748
542	/*****************************************************************************/	749	/*****************************************************************************/
543		750
544	/* ECB_NO_THREADS - ecb is not used by multiple threads, ever */	751	/* ECB_NO_THREADS - ecb is not used by multiple threads, ever */
545	/* ECB_NO_SMP - ecb might be used in multiple threads, but only on a single cpu */	752	/* ECB_NO_SMP - ecb might be used in multiple threads, but only on a single cpu */
546		753
547	#if ECB_NO_THREADS	754	#if ECB_NO_THREADS
548	# define ECB_NO_SMP 1	755	#define ECB_NO_SMP 1
549	#endif	756	#endif
550		757
551	#if ECB_NO_THREADS || ECB_NO_SMP	758	#if ECB_NO_SMP
552	#define ECB_MEMORY_FENCE do { } while (0)	759	#define ECB_MEMORY_FENCE do { } while (0)
		760	#endif
		761
		762	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/compiler_ref/compiler_builtins.html */
		763	#if __xlC__ && ECB_CPP
		764	#include <builtins.h>
		765	#endif
		766
		767	#if 1400 <= _MSC_VER
		768	#include <intrin.h> /* fence functions _ReadBarrier, also bit search functions _BitScanReverse */
553	#endif	769	#endif
554		770
555	#ifndef ECB_MEMORY_FENCE	771	#ifndef ECB_MEMORY_FENCE
556	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	772	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
		773	#define ECB_MEMORY_FENCE_RELAXED __asm__ __volatile__ ("" : : : "memory")
557	#if __i386 || __i386__	774	#if __i386 || __i386__
558	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")	775	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")
559	#define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE /* non-lock xchg might be enough */	776	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
560	#define ECB_MEMORY_FENCE_RELEASE do { } while (0) /* unlikely to change in future cpus */	777	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
561	#elif __amd64 || __amd64__ || __x86_64 || __x86_64__	778	#elif ECB_GCC_AMD64
562	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")	779	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")
563	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("lfence" : : : "memory")	780	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
564	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("sfence") /* play safe - not needed in any current cpu */	781	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
565	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__	782	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__
566	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")	783	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")
		784	#elif defined __ARM_ARCH_2__ \
		785	|| defined __ARM_ARCH_3__ || defined __ARM_ARCH_3M__ \
		786	|| defined __ARM_ARCH_4__ || defined __ARM_ARCH_4T__ \
		787	|| defined __ARM_ARCH_5__ || defined __ARM_ARCH_5E__ \
		788	|| defined __ARM_ARCH_5T__ || defined __ARM_ARCH_5TE__ \
		789	|| defined __ARM_ARCH_5TEJ__
		790	/* should not need any, unless running old code on newer cpu - arm doesn't support that */
567	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \	791	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \
568	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__	792	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__ \
		793	|| defined __ARM_ARCH_6T2__
569	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")	794	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")
570	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \	795	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \
571	|| defined __ARM_ARCH_7M__ || defined __ARM_ARCH_7R__	796	|| defined __ARM_ARCH_7R__ || defined __ARM_ARCH_7M__
572	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")	797	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")
573	#elif __sparc || __sparc__	798	#elif __aarch64__
		799	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb ish" : : : "memory")
		800	#elif (__sparc || __sparc__) && !(__sparc_v8__ || defined __sparcv8)
574	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad | " : : : "memory")	801	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")
575	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")	802	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")
576	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")	803	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")
577	#elif defined __s390__ || defined __s390x__	804	#elif defined __s390__ || defined __s390x__
578	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")	805	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")
579	#elif defined __mips__	806	#elif defined __mips__
		807	/* GNU/Linux emulates sync on mips1 architectures, so we force its use */
		808	/* anybody else who still uses mips1 is supposed to send in their version, with detection code. */
580	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")	809	#define ECB_MEMORY_FENCE __asm__ __volatile__ (".set mips2; sync; .set mips0" : : : "memory")
581	#elif defined __alpha__	810	#elif defined __alpha__
582	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mb" : : : "memory")	811	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mb" : : : "memory")
		812	#elif defined __hppa__
		813	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("" : : : "memory")
		814	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")
		815	#elif defined __ia64__
		816	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mf" : : : "memory")
		817	#elif defined __m68k__
		818	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("" : : : "memory")
		819	#elif defined __m88k__
		820	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("tb1 0,%%r0,128" : : : "memory")
		821	#elif defined __sh__
		822	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("" : : : "memory")
583	#endif	823	#endif
584	#endif	824	#endif
585	#endif	825	#endif
586		826
587	#ifndef ECB_MEMORY_FENCE	827	#ifndef ECB_MEMORY_FENCE
		828	#if ECB_GCC_VERSION(4,7)
		829	/* see comment below (stdatomic.h) about the C11 memory model. */
		830	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)
		831	#define ECB_MEMORY_FENCE_ACQUIRE __atomic_thread_fence (__ATOMIC_ACQUIRE)
		832	#define ECB_MEMORY_FENCE_RELEASE __atomic_thread_fence (__ATOMIC_RELEASE)
		833	#define ECB_MEMORY_FENCE_RELAXED __atomic_thread_fence (__ATOMIC_RELAXED)
		834
		835	#elif ECB_CLANG_EXTENSION(c_atomic)
		836	/* see comment below (stdatomic.h) about the C11 memory model. */
		837	#define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)
		838	#define ECB_MEMORY_FENCE_ACQUIRE __c11_atomic_thread_fence (__ATOMIC_ACQUIRE)
		839	#define ECB_MEMORY_FENCE_RELEASE __c11_atomic_thread_fence (__ATOMIC_RELEASE)
		840	#define ECB_MEMORY_FENCE_RELAXED __c11_atomic_thread_fence (__ATOMIC_RELAXED)
		841
588	#if ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__	842	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__
589	#define ECB_MEMORY_FENCE __sync_synchronize ()	843	#define ECB_MEMORY_FENCE __sync_synchronize ()
590	/*#define ECB_MEMORY_FENCE_ACQUIRE ({ char dummy = 0; __sync_lock_test_and_set (&dummy, 1); }) */	844	#elif _MSC_VER >= 1500 /* VC++ 2008 */
591	/*#define ECB_MEMORY_FENCE_RELEASE ({ char dummy = 1; __sync_lock_release (&dummy ); }) */	845	/* apparently, microsoft broke all the memory barrier stuff in Visual Studio 2008... */
		846	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)
		847	#define ECB_MEMORY_FENCE _ReadWriteBarrier (); MemoryBarrier()
		848	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier (); MemoryBarrier() /* according to msdn, _ReadBarrier is not a load fence */
		849	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier (); MemoryBarrier()
592	#elif _MSC_VER >= 1400 /* VC++ 2005 */	850	#elif _MSC_VER >= 1400 /* VC++ 2005 */
593	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)	851	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)
594	#define ECB_MEMORY_FENCE _ReadWriteBarrier ()	852	#define ECB_MEMORY_FENCE _ReadWriteBarrier ()
595	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier () /* according to msdn, _ReadBarrier is not a load fence */	853	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier () /* according to msdn, _ReadBarrier is not a load fence */
596	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier ()	854	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier ()
597	#elif defined _WIN32	855	#elif defined _WIN32
598	#include <WinNT.h>	856	#include <WinNT.h>
599	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */	857	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */
600	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	858	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
601	#include <mbarrier.h>	859	#include <mbarrier.h>
602	#define ECB_MEMORY_FENCE __machine_rw_barrier ()	860	#define ECB_MEMORY_FENCE __machine_rw_barrier ()
603	#define ECB_MEMORY_FENCE_ACQUIRE __machine_r_barrier ()	861	#define ECB_MEMORY_FENCE_ACQUIRE __machine_acq_barrier ()
604	#define ECB_MEMORY_FENCE_RELEASE __machine_w_barrier ()	862	#define ECB_MEMORY_FENCE_RELEASE __machine_rel_barrier ()
		863	#define ECB_MEMORY_FENCE_RELAXED __compiler_barrier ()
605	#elif __xlC__	864	#elif __xlC__
606	#define ECB_MEMORY_FENCE __sync ()	865	#define ECB_MEMORY_FENCE __sync ()
		866	#endif
		867	#endif
		868
		869	#ifndef ECB_MEMORY_FENCE
		870	#if ECB_C11 && !defined __STDC_NO_ATOMICS__
		871	/* we assume that these memory fences work on all variables/all memory accesses, */
		872	/* not just C11 atomics and atomic accesses */
		873	#include <stdatomic.h>
		874	#define ECB_MEMORY_FENCE atomic_thread_fence (memory_order_seq_cst)
		875	#define ECB_MEMORY_FENCE_ACQUIRE atomic_thread_fence (memory_order_acquire)
		876	#define ECB_MEMORY_FENCE_RELEASE atomic_thread_fence (memory_order_release)
607	#endif	877	#endif
608	#endif	878	#endif
609		879
610	#ifndef ECB_MEMORY_FENCE	880	#ifndef ECB_MEMORY_FENCE
611	#if !ECB_AVOID_PTHREADS	881	#if !ECB_AVOID_PTHREADS
…		…
631		901
632	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE	902	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE
633	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	903	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
634	#endif	904	#endif
635		905
		906	#if !defined ECB_MEMORY_FENCE_RELAXED && defined ECB_MEMORY_FENCE
		907	#define ECB_MEMORY_FENCE_RELAXED ECB_MEMORY_FENCE /* very heavy-handed */
		908	#endif
		909
636	/*****************************************************************************/	910	/*****************************************************************************/
637		911
638	#define ECB_C99 (__STDC_VERSION__ >= 199901L)	912	#if ECB_CPP
639
640	#if __cplusplus
641	#define ecb_inline static inline	913	#define ecb_inline static inline
642	#elif ECB_GCC_VERSION(2,5)	914	#elif ECB_GCC_VERSION(2,5)
643	#define ecb_inline static __inline__	915	#define ecb_inline static __inline__
644	#elif ECB_C99	916	#elif ECB_C99
645	#define ecb_inline static inline	917	#define ecb_inline static inline
…		…
659		931
660	#define ECB_CONCAT_(a, b) a ## b	932	#define ECB_CONCAT_(a, b) a ## b
661	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)	933	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)
662	#define ECB_STRINGIFY_(a) # a	934	#define ECB_STRINGIFY_(a) # a
663	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)	935	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)
		936	#define ECB_STRINGIFY_EXPR(expr) ((expr), ECB_STRINGIFY_ (expr))
664		937
665	#define ecb_function_ ecb_inline	938	#define ecb_function_ ecb_inline
666		939
667	#if ECB_GCC_VERSION(3,1)	940	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_VERSION(2,8)
668	#define ecb_attribute(attrlist) __attribute__(attrlist)	941	#define ecb_attribute(attrlist) __attribute__ (attrlist)
		942	#else
		943	#define ecb_attribute(attrlist)
		944	#endif
		945
		946	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_constant_p)
669	#define ecb_is_constant(expr) __builtin_constant_p (expr)	947	#define ecb_is_constant(expr) __builtin_constant_p (expr)
		948	#else
		949	/* possible C11 impl for integral types
		950	typedef struct ecb_is_constant_struct ecb_is_constant_struct;
		951	#define ecb_is_constant(expr) _Generic ((1 ? (struct ecb_is_constant_struct *)0 : (void *)((expr) - (expr)), ecb_is_constant_struct *: 0, default: 1)) */
		952
		953	#define ecb_is_constant(expr) 0
		954	#endif
		955
		956	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_expect)
670	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))	957	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))
		958	#else
		959	#define ecb_expect(expr,value) (expr)
		960	#endif
		961
		962	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_prefetch)
671	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)	963	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)
672	#else	964	#else
673	#define ecb_attribute(attrlist)
674	#define ecb_is_constant(expr) 0
675	#define ecb_expect(expr,value) (expr)
676	#define ecb_prefetch(addr,rw,locality)	965	#define ecb_prefetch(addr,rw,locality)
677	#endif	966	#endif
678		967
679	/* no emulation for ecb_decltype */	968	/* no emulation for ecb_decltype */
680	#if ECB_GCC_VERSION(4,5)	969	#if ECB_CPP11
		970	// older implementations might have problems with decltype(x)::type, work around it
		971	template<class T> struct ecb_decltype_t { typedef T type; };
681	#define ecb_decltype(x) __decltype(x)	972	#define ecb_decltype(x) ecb_decltype_t<decltype (x)>::type
682	#elif ECB_GCC_VERSION(3,0)	973	#elif ECB_GCC_VERSION(3,0) || ECB_CLANG_VERSION(2,8)
683	#define ecb_decltype(x) __typeof(x)	974	#define ecb_decltype(x) __typeof__ (x)
684	#endif	975	#endif
685		976
		977	#if _MSC_VER >= 1300
		978	#define ecb_deprecated __declspec (deprecated)
		979	#else
		980	#define ecb_deprecated ecb_attribute ((__deprecated__))
		981	#endif
		982
		983	#if _MSC_VER >= 1500
		984	#define ecb_deprecated_message(msg) __declspec (deprecated (msg))
		985	#elif ECB_GCC_VERSION(4,5)
		986	#define ecb_deprecated_message(msg) ecb_attribute ((__deprecated__ (msg))
		987	#else
		988	#define ecb_deprecated_message(msg) ecb_deprecated
		989	#endif
		990
		991	#if _MSC_VER >= 1400
		992	#define ecb_noinline __declspec (noinline)
		993	#else
686	#define ecb_noinline ecb_attribute ((__noinline__))	994	#define ecb_noinline ecb_attribute ((__noinline__))
687	#define ecb_noreturn ecb_attribute ((__noreturn__))	995	#endif
		996
688	#define ecb_unused ecb_attribute ((__unused__))	997	#define ecb_unused ecb_attribute ((__unused__))
689	#define ecb_const ecb_attribute ((__const__))	998	#define ecb_const ecb_attribute ((__const__))
690	#define ecb_pure ecb_attribute ((__pure__))	999	#define ecb_pure ecb_attribute ((__pure__))
		1000
		1001	#if ECB_C11 || __IBMC_NORETURN
		1002	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/language_ref/noreturn.html */
		1003	#define ecb_noreturn _Noreturn
		1004	#elif ECB_CPP11
		1005	#define ecb_noreturn [[noreturn]]
		1006	#elif _MSC_VER >= 1200
		1007	/* http://msdn.microsoft.com/en-us/library/k6ktzx3s.aspx */
		1008	#define ecb_noreturn __declspec (noreturn)
		1009	#else
		1010	#define ecb_noreturn ecb_attribute ((__noreturn__))
		1011	#endif
691		1012
692	#if ECB_GCC_VERSION(4,3)	1013	#if ECB_GCC_VERSION(4,3)
693	#define ecb_artificial ecb_attribute ((__artificial__))	1014	#define ecb_artificial ecb_attribute ((__artificial__))
694	#define ecb_hot ecb_attribute ((__hot__))	1015	#define ecb_hot ecb_attribute ((__hot__))
695	#define ecb_cold ecb_attribute ((__cold__))	1016	#define ecb_cold ecb_attribute ((__cold__))
…		…
707	/* for compatibility to the rest of the world */	1028	/* for compatibility to the rest of the world */
708	#define ecb_likely(expr) ecb_expect_true (expr)	1029	#define ecb_likely(expr) ecb_expect_true (expr)
709	#define ecb_unlikely(expr) ecb_expect_false (expr)	1030	#define ecb_unlikely(expr) ecb_expect_false (expr)
710		1031
711	/* count trailing zero bits and count # of one bits */	1032	/* count trailing zero bits and count # of one bits */
712	#if ECB_GCC_VERSION(3,4)	1033	#if ECB_GCC_VERSION(3,4) \
		1034	|| (ECB_CLANG_BUILTIN(__builtin_clz) && ECB_CLANG_BUILTIN(__builtin_clzll) \
		1035	&& ECB_CLANG_BUILTIN(__builtin_ctz) && ECB_CLANG_BUILTIN(__builtin_ctzll) \
		1036	&& ECB_CLANG_BUILTIN(__builtin_popcount))
713	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */	1037	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */
714	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)	1038	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)
715	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)	1039	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)
716	#define ecb_ctz32(x) __builtin_ctz (x)	1040	#define ecb_ctz32(x) __builtin_ctz (x)
717	#define ecb_ctz64(x) __builtin_ctzll (x)	1041	#define ecb_ctz64(x) __builtin_ctzll (x)
718	#define ecb_popcount32(x) __builtin_popcount (x)	1042	#define ecb_popcount32(x) __builtin_popcount (x)
719	/* no popcountll */	1043	/* no popcountll */
720	#else	1044	#else
721	ecb_function_ int ecb_ctz32 (uint32_t x) ecb_const;	1045	ecb_function_ ecb_const int ecb_ctz32 (uint32_t x);
722	ecb_function_ int	1046	ecb_function_ ecb_const int
723	ecb_ctz32 (uint32_t x)	1047	ecb_ctz32 (uint32_t x)
724	{	1048	{
		1049	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		1050	unsigned long r;
		1051	_BitScanForward (&r, x);
		1052	return (int)r;
		1053	#else
725	int r = 0;	1054	int r = 0;
726		1055
727	x &= ~x + 1; /* this isolates the lowest bit */	1056	x &= ~x + 1; /* this isolates the lowest bit */
728		1057
729	#if ECB_branchless_on_i386	1058	#if ECB_branchless_on_i386
…		…
739	if (x & 0xff00ff00) r += 8;	1068	if (x & 0xff00ff00) r += 8;
740	if (x & 0xffff0000) r += 16;	1069	if (x & 0xffff0000) r += 16;
741	#endif	1070	#endif
742		1071
743	return r;	1072	return r;
		1073	#endif
744	}	1074	}
745		1075
746	ecb_function_ int ecb_ctz64 (uint64_t x) ecb_const;	1076	ecb_function_ ecb_const int ecb_ctz64 (uint64_t x);
747	ecb_function_ int	1077	ecb_function_ ecb_const int
748	ecb_ctz64 (uint64_t x)	1078	ecb_ctz64 (uint64_t x)
749	{	1079	{
		1080	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1081	unsigned long r;
		1082	_BitScanForward64 (&r, x);
		1083	return (int)r;
		1084	#else
750	int shift = x & 0xffffffffU ? 0 : 32;	1085	int shift = x & 0xffffffff ? 0 : 32;
751	return ecb_ctz32 (x >> shift) + shift;	1086	return ecb_ctz32 (x >> shift) + shift;
		1087	#endif
752	}	1088	}
753		1089
754	ecb_function_ int ecb_popcount32 (uint32_t x) ecb_const;	1090	ecb_function_ ecb_const int ecb_popcount32 (uint32_t x);
755	ecb_function_ int	1091	ecb_function_ ecb_const int
756	ecb_popcount32 (uint32_t x)	1092	ecb_popcount32 (uint32_t x)
757	{	1093	{
758	x -= (x >> 1) & 0x55555555;	1094	x -= (x >> 1) & 0x55555555;
759	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);	1095	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);
760	x = ((x >> 4) + x) & 0x0f0f0f0f;	1096	x = ((x >> 4) + x) & 0x0f0f0f0f;
761	x *= 0x01010101;	1097	x *= 0x01010101;
762		1098
763	return x >> 24;	1099	return x >> 24;
764	}	1100	}
765		1101
766	ecb_function_ int ecb_ld32 (uint32_t x) ecb_const;	1102	ecb_function_ ecb_const int ecb_ld32 (uint32_t x);
767	ecb_function_ int ecb_ld32 (uint32_t x)	1103	ecb_function_ ecb_const int ecb_ld32 (uint32_t x)
768	{	1104	{
		1105	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		1106	unsigned long r;
		1107	_BitScanReverse (&r, x);
		1108	return (int)r;
		1109	#else
769	int r = 0;	1110	int r = 0;
770		1111
771	if (x >> 16) { x >>= 16; r += 16; }	1112	if (x >> 16) { x >>= 16; r += 16; }
772	if (x >> 8) { x >>= 8; r += 8; }	1113	if (x >> 8) { x >>= 8; r += 8; }
773	if (x >> 4) { x >>= 4; r += 4; }	1114	if (x >> 4) { x >>= 4; r += 4; }
774	if (x >> 2) { x >>= 2; r += 2; }	1115	if (x >> 2) { x >>= 2; r += 2; }
775	if (x >> 1) { r += 1; }	1116	if (x >> 1) { r += 1; }
776		1117
777	return r;	1118	return r;
		1119	#endif
778	}	1120	}
779		1121
780	ecb_function_ int ecb_ld64 (uint64_t x) ecb_const;	1122	ecb_function_ ecb_const int ecb_ld64 (uint64_t x);
781	ecb_function_ int ecb_ld64 (uint64_t x)	1123	ecb_function_ ecb_const int ecb_ld64 (uint64_t x)
782	{	1124	{
		1125	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1126	unsigned long r;
		1127	_BitScanReverse64 (&r, x);
		1128	return (int)r;
		1129	#else
783	int r = 0;	1130	int r = 0;
784		1131
785	if (x >> 32) { x >>= 32; r += 32; }	1132	if (x >> 32) { x >>= 32; r += 32; }
786		1133
787	return r + ecb_ld32 (x);	1134	return r + ecb_ld32 (x);
		1135	#endif
788	}	1136	}
789	#endif	1137	#endif
790		1138
		1139	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x);
		1140	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x) { return !(x & (x - 1)); }
		1141	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x);
		1142	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x) { return !(x & (x - 1)); }
		1143
791	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x) ecb_const;	1144	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x);
792	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x)	1145	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x)
793	{	1146	{
794	return ( (x * 0x0802U & 0x22110U)	1147	return ( (x * 0x0802U & 0x22110U)
795	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;	1148	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;
796	}	1149	}
797		1150
798	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x) ecb_const;	1151	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x);
799	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x)	1152	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x)
800	{	1153	{
801	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);	1154	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);
802	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);	1155	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);
803	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);	1156	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);
804	x = ( x >> 8 ) | ( x << 8);	1157	x = ( x >> 8 ) | ( x << 8);
805		1158
806	return x;	1159	return x;
807	}	1160	}
808		1161
809	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x) ecb_const;	1162	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x);
810	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x)	1163	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x)
811	{	1164	{
812	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);	1165	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);
813	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);	1166	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);
814	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);	1167	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);
815	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);	1168	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);
…		…
818	return x;	1171	return x;
819	}	1172	}
820		1173
821	/* popcount64 is only available on 64 bit cpus as gcc builtin */	1174	/* popcount64 is only available on 64 bit cpus as gcc builtin */
822	/* so for this version we are lazy */	1175	/* so for this version we are lazy */
823	ecb_function_ int ecb_popcount64 (uint64_t x) ecb_const;	1176	ecb_function_ ecb_const int ecb_popcount64 (uint64_t x);
824	ecb_function_ int	1177	ecb_function_ ecb_const int
825	ecb_popcount64 (uint64_t x)	1178	ecb_popcount64 (uint64_t x)
826	{	1179	{
827	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);	1180	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);
828	}	1181	}
829		1182
830	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) ecb_const;	1183	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count);
831	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) ecb_const;	1184	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count);
832	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) ecb_const;	1185	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count);
833	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) ecb_const;	1186	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count);
834	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) ecb_const;	1187	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count);
835	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) ecb_const;	1188	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count);
836	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) ecb_const;	1189	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count);
837	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) ecb_const;	1190	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count);
838		1191
839	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }	1192	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }
840	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }	1193	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }
841	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }	1194	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }
842	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }	1195	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }
843	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }	1196	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }
844	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }	1197	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }
845	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }	1198	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }
846	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }	1199	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }
847		1200
848	#if ECB_GCC_VERSION(4,3)	1201	#if ECB_GCC_VERSION(4,3) || (ECB_CLANG_BUILTIN(__builtin_bswap32) && ECB_CLANG_BUILTIN(__builtin_bswap64))
		1202	#if ECB_GCC_VERSION(4,8) || ECB_CLANG_BUILTIN(__builtin_bswap16)
		1203	#define ecb_bswap16(x) __builtin_bswap16 (x)
		1204	#else
849	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)	1205	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)
		1206	#endif
850	#define ecb_bswap32(x) __builtin_bswap32 (x)	1207	#define ecb_bswap32(x) __builtin_bswap32 (x)
851	#define ecb_bswap64(x) __builtin_bswap64 (x)	1208	#define ecb_bswap64(x) __builtin_bswap64 (x)
		1209	#elif _MSC_VER
		1210	#include <stdlib.h>
		1211	#define ecb_bswap16(x) ((uint16_t)_byteswap_ushort ((uint16_t)(x)))
		1212	#define ecb_bswap32(x) ((uint32_t)_byteswap_ulong ((uint32_t)(x)))
		1213	#define ecb_bswap64(x) ((uint64_t)_byteswap_uint64 ((uint64_t)(x)))
852	#else	1214	#else
853	ecb_function_ uint16_t ecb_bswap16 (uint16_t x) ecb_const;	1215	ecb_function_ ecb_const uint16_t ecb_bswap16 (uint16_t x);
854	ecb_function_ uint16_t	1216	ecb_function_ ecb_const uint16_t
855	ecb_bswap16 (uint16_t x)	1217	ecb_bswap16 (uint16_t x)
856	{	1218	{
857	return ecb_rotl16 (x, 8);	1219	return ecb_rotl16 (x, 8);
858	}	1220	}
859		1221
860	ecb_function_ uint32_t ecb_bswap32 (uint32_t x) ecb_const;	1222	ecb_function_ ecb_const uint32_t ecb_bswap32 (uint32_t x);
861	ecb_function_ uint32_t	1223	ecb_function_ ecb_const uint32_t
862	ecb_bswap32 (uint32_t x)	1224	ecb_bswap32 (uint32_t x)
863	{	1225	{
864	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);	1226	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);
865	}	1227	}
866		1228
867	ecb_function_ uint64_t ecb_bswap64 (uint64_t x) ecb_const;	1229	ecb_function_ ecb_const uint64_t ecb_bswap64 (uint64_t x);
868	ecb_function_ uint64_t	1230	ecb_function_ ecb_const uint64_t
869	ecb_bswap64 (uint64_t x)	1231	ecb_bswap64 (uint64_t x)
870	{	1232	{
871	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);	1233	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);
872	}	1234	}
873	#endif	1235	#endif
874		1236
875	#if ECB_GCC_VERSION(4,5)	1237	#if ECB_GCC_VERSION(4,5) || ECB_CLANG_BUILTIN(__builtin_unreachable)
876	#define ecb_unreachable() __builtin_unreachable ()	1238	#define ecb_unreachable() __builtin_unreachable ()
877	#else	1239	#else
878	/* this seems to work fine, but gcc always emits a warning for it :/ */	1240	/* this seems to work fine, but gcc always emits a warning for it :/ */
879	ecb_inline void ecb_unreachable (void) ecb_noreturn;	1241	ecb_inline ecb_noreturn void ecb_unreachable (void);
880	ecb_inline void ecb_unreachable (void) { }	1242	ecb_inline ecb_noreturn void ecb_unreachable (void) { }
881	#endif	1243	#endif
882		1244
883	/* try to tell the compiler that some condition is definitely true */	1245	/* try to tell the compiler that some condition is definitely true */
884	#define ecb_assume(cond) do { if (!(cond)) ecb_unreachable (); } while (0)	1246	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0
885		1247
886	ecb_inline unsigned char ecb_byteorder_helper (void) ecb_const;	1248	ecb_inline ecb_const uint32_t ecb_byteorder_helper (void);
887	ecb_inline unsigned char	1249	ecb_inline ecb_const uint32_t
888	ecb_byteorder_helper (void)	1250	ecb_byteorder_helper (void)
889	{	1251	{
890	const uint32_t u = 0x11223344;	1252	/* the union code still generates code under pressure in gcc, */
891	return *(unsigned char *)&u;	1253	/* but less than using pointers, and always seems to */
		1254	/* successfully return a constant. */
		1255	/* the reason why we have this horrible preprocessor mess */
		1256	/* is to avoid it in all cases, at least on common architectures */
		1257	/* or when using a recent enough gcc version (>= 4.6) */
		1258	#if (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_LITTLE_ENDIAN__) \
		1259	|| ((__i386 || __i386__ || _M_IX86 || ECB_GCC_AMD64 || ECB_MSVC_AMD64) && !__VOS__)
		1260	#define ECB_LITTLE_ENDIAN 1
		1261	return 0x44332211;
		1262	#elif (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__) \
		1263	|| ((__AARCH64EB__ || __MIPSEB__ || __ARMEB__) && !__VOS__)
		1264	#define ECB_BIG_ENDIAN 1
		1265	return 0x11223344;
		1266	#else
		1267	union
		1268	{
		1269	uint8_t c[4];
		1270	uint32_t u;
		1271	} u = { 0x11, 0x22, 0x33, 0x44 };
		1272	return u.u;
		1273	#endif
892	}	1274	}
893		1275
894	ecb_inline ecb_bool ecb_big_endian (void) ecb_const;	1276	ecb_inline ecb_const ecb_bool ecb_big_endian (void);
895	ecb_inline ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11; }	1277	ecb_inline ecb_const ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11223344; }
896	ecb_inline ecb_bool ecb_little_endian (void) ecb_const;	1278	ecb_inline ecb_const ecb_bool ecb_little_endian (void);
897	ecb_inline ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44; }	1279	ecb_inline ecb_const ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44332211; }
898		1280
899	#if ECB_GCC_VERSION(3,0) || ECB_C99	1281	#if ECB_GCC_VERSION(3,0) || ECB_C99
900	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))	1282	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))
901	#else	1283	#else
902	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))	1284	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))
903	#endif	1285	#endif
904		1286
905	#if __cplusplus	1287	#if ECB_CPP
906	template<typename T>	1288	template<typename T>
907	static inline T ecb_div_rd (T val, T div)	1289	static inline T ecb_div_rd (T val, T div)
908	{	1290	{
909	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;	1291	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;
910	}	1292	}
…		…
927	}	1309	}
928	#else	1310	#else
929	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))	1311	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))
930	#endif	1312	#endif
931		1313
		1314	ecb_function_ ecb_const uint32_t ecb_binary16_to_binary32 (uint32_t x);
		1315	ecb_function_ ecb_const uint32_t
		1316	ecb_binary16_to_binary32 (uint32_t x)
		1317	{
		1318	unsigned int s = (x & 0x8000) << (31 - 15);
		1319	int e = (x >> 10) & 0x001f;
		1320	unsigned int m = x & 0x03ff;
		1321
		1322	if (ecb_expect_false (e == 31))
		1323	/* infinity or NaN */
		1324	e = 255 - (127 - 15);
		1325	else if (ecb_expect_false (!e))
		1326	{
		1327	if (ecb_expect_true (!m))
		1328	/* zero, handled by code below by forcing e to 0 */
		1329	e = 0 - (127 - 15);
		1330	else
		1331	{
		1332	/* subnormal, renormalise */
		1333	unsigned int s = 10 - ecb_ld32 (m);
		1334
		1335	m = (m << s) & 0x3ff; /* mask implicit bit */
		1336	e -= s - 1;
		1337	}
		1338	}
		1339
		1340	/* e and m now are normalised, or zero, (or inf or nan) */
		1341	e += 127 - 15;
		1342
		1343	return s | (e << 23) | (m << (23 - 10));
		1344	}
		1345
		1346	ecb_function_ ecb_const uint16_t ecb_binary32_to_binary16 (uint32_t x);
		1347	ecb_function_ ecb_const uint16_t
		1348	ecb_binary32_to_binary16 (uint32_t x)
		1349	{
		1350	unsigned int s = (x >> 16) & 0x00008000; /* sign bit, the easy part */
		1351	unsigned int e = ((x >> 23) & 0x000000ff) - (127 - 15); /* the desired exponent */
		1352	unsigned int m = x & 0x007fffff;
		1353
		1354	x &= 0x7fffffff;
		1355
		1356	/* if it's within range of binary16 normals, use fast path */
		1357	if (ecb_expect_true (0x38800000 <= x && x <= 0x477fefff))
		1358	{
		1359	/* mantissa round-to-even */
		1360	m += 0x00000fff + ((m >> (23 - 10)) & 1);
		1361
		1362	/* handle overflow */
		1363	if (ecb_expect_false (m >= 0x00800000))
		1364	{
		1365	m >>= 1;
		1366	e += 1;
		1367	}
		1368
		1369	return s | (e << 10) | (m >> (23 - 10));
		1370	}
		1371
		1372	/* handle large numbers and infinity */
		1373	if (ecb_expect_true (0x477fefff < x && x <= 0x7f800000))
		1374	return s | 0x7c00;
		1375
		1376	/* handle zero, subnormals and small numbers */
		1377	if (ecb_expect_true (x < 0x38800000))
		1378	{
		1379	/* zero */
		1380	if (ecb_expect_true (!x))
		1381	return s;
		1382
		1383	/* handle subnormals */
		1384
		1385	/* too small, will be zero */
		1386	if (e < (14 - 24)) /* might not be sharp, but is good enough */
		1387	return s;
		1388
		1389	m |= 0x00800000; /* make implicit bit explicit */
		1390
		1391	/* very tricky - we need to round to the nearest e (+10) bit value */
		1392	{
		1393	unsigned int bits = 14 - e;
		1394	unsigned int half = (1 << (bits - 1)) - 1;
		1395	unsigned int even = (m >> bits) & 1;
		1396
		1397	/* if this overflows, we will end up with a normalised number */
		1398	m = (m + half + even) >> bits;
		1399	}
		1400
		1401	return s | m;
		1402	}
		1403
		1404	/* handle NaNs, preserve leftmost nan bits, but make sure we don't turn them into infinities */
		1405	m >>= 13;
		1406
		1407	return s | 0x7c00 | m | !m;
		1408	}
		1409
		1410	/*******************************************************************************/
		1411	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */
		1412
		1413	/* basically, everything uses "ieee pure-endian" floating point numbers */
		1414	/* the only noteworthy exception is ancient armle, which uses order 43218765 */
		1415	#if 0 \
		1416	|| __i386 || __i386__ \
		1417	|| ECB_GCC_AMD64 \
		1418	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \
		1419	|| defined __s390__ || defined __s390x__ \
		1420	|| defined __mips__ \
		1421	|| defined __alpha__ \
		1422	|| defined __hppa__ \
		1423	|| defined __ia64__ \
		1424	|| defined __m68k__ \
		1425	|| defined __m88k__ \
		1426	|| defined __sh__ \
		1427	|| defined _M_IX86 || defined ECB_MSVC_AMD64 || defined _M_IA64 \
		1428	|| (defined __arm__ && (defined __ARM_EABI__ || defined __EABI__ || defined __VFP_FP__ || defined _WIN32_WCE || defined __ANDROID__)) \
		1429	|| defined __aarch64__
		1430	#define ECB_STDFP 1
		1431	#include <string.h> /* for memcpy */
		1432	#else
		1433	#define ECB_STDFP 0
		1434	#endif
		1435
		1436	#ifndef ECB_NO_LIBM
		1437
		1438	#include <math.h> /* for frexp*, ldexp*, INFINITY, NAN */
		1439
		1440	/* only the oldest of old doesn't have this one. solaris. */
		1441	#ifdef INFINITY
		1442	#define ECB_INFINITY INFINITY
		1443	#else
		1444	#define ECB_INFINITY HUGE_VAL
		1445	#endif
		1446
		1447	#ifdef NAN
		1448	#define ECB_NAN NAN
		1449	#else
		1450	#define ECB_NAN ECB_INFINITY
		1451	#endif
		1452
		1453	#if ECB_C99 || _XOPEN_VERSION >= 600 || _POSIX_VERSION >= 200112L
		1454	#define ecb_ldexpf(x,e) ldexpf ((x), (e))
		1455	#define ecb_frexpf(x,e) frexpf ((x), (e))
		1456	#else
		1457	#define ecb_ldexpf(x,e) (float) ldexp ((double) (x), (e))
		1458	#define ecb_frexpf(x,e) (float) frexp ((double) (x), (e))
		1459	#endif
		1460
		1461	/* convert a float to ieee single/binary32 */
		1462	ecb_function_ ecb_const uint32_t ecb_float_to_binary32 (float x);
		1463	ecb_function_ ecb_const uint32_t
		1464	ecb_float_to_binary32 (float x)
		1465	{
		1466	uint32_t r;
		1467
		1468	#if ECB_STDFP
		1469	memcpy (&r, &x, 4);
		1470	#else
		1471	/* slow emulation, works for anything but -0 */
		1472	uint32_t m;
		1473	int e;
		1474
		1475	if (x == 0e0f ) return 0x00000000U;
		1476	if (x > +3.40282346638528860e+38f) return 0x7f800000U;
		1477	if (x < -3.40282346638528860e+38f) return 0xff800000U;
		1478	if (x != x ) return 0x7fbfffffU;
		1479
		1480	m = ecb_frexpf (x, &e) * 0x1000000U;
		1481
		1482	r = m & 0x80000000U;
		1483
		1484	if (r)
		1485	m = -m;
		1486
		1487	if (e <= -126)
		1488	{
		1489	m &= 0xffffffU;
		1490	m >>= (-125 - e);
		1491	e = -126;
		1492	}
		1493
		1494	r |= (e + 126) << 23;
		1495	r |= m & 0x7fffffU;
		1496	#endif
		1497
		1498	return r;
		1499	}
		1500
		1501	/* converts an ieee single/binary32 to a float */
		1502	ecb_function_ ecb_const float ecb_binary32_to_float (uint32_t x);
		1503	ecb_function_ ecb_const float
		1504	ecb_binary32_to_float (uint32_t x)
		1505	{
		1506	float r;
		1507
		1508	#if ECB_STDFP
		1509	memcpy (&r, &x, 4);
		1510	#else
		1511	/* emulation, only works for normals and subnormals and +0 */
		1512	int neg = x >> 31;
		1513	int e = (x >> 23) & 0xffU;
		1514
		1515	x &= 0x7fffffU;
		1516
		1517	if (e)
		1518	x |= 0x800000U;
		1519	else
		1520	e = 1;
		1521
		1522	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */
		1523	r = ecb_ldexpf (x * (0.5f / 0x800000U), e - 126);
		1524
		1525	r = neg ? -r : r;
		1526	#endif
		1527
		1528	return r;
		1529	}
		1530
		1531	/* convert a double to ieee double/binary64 */
		1532	ecb_function_ ecb_const uint64_t ecb_double_to_binary64 (double x);
		1533	ecb_function_ ecb_const uint64_t
		1534	ecb_double_to_binary64 (double x)
		1535	{
		1536	uint64_t r;
		1537
		1538	#if ECB_STDFP
		1539	memcpy (&r, &x, 8);
		1540	#else
		1541	/* slow emulation, works for anything but -0 */
		1542	uint64_t m;
		1543	int e;
		1544
		1545	if (x == 0e0 ) return 0x0000000000000000U;
		1546	if (x > +1.79769313486231470e+308) return 0x7ff0000000000000U;
		1547	if (x < -1.79769313486231470e+308) return 0xfff0000000000000U;
		1548	if (x != x ) return 0X7ff7ffffffffffffU;
		1549
		1550	m = frexp (x, &e) * 0x20000000000000U;
		1551
		1552	r = m & 0x8000000000000000;;
		1553
		1554	if (r)
		1555	m = -m;
		1556
		1557	if (e <= -1022)
		1558	{
		1559	m &= 0x1fffffffffffffU;
		1560	m >>= (-1021 - e);
		1561	e = -1022;
		1562	}
		1563
		1564	r |= ((uint64_t)(e + 1022)) << 52;
		1565	r |= m & 0xfffffffffffffU;
		1566	#endif
		1567
		1568	return r;
		1569	}
		1570
		1571	/* converts an ieee double/binary64 to a double */
		1572	ecb_function_ ecb_const double ecb_binary64_to_double (uint64_t x);
		1573	ecb_function_ ecb_const double
		1574	ecb_binary64_to_double (uint64_t x)
		1575	{
		1576	double r;
		1577
		1578	#if ECB_STDFP
		1579	memcpy (&r, &x, 8);
		1580	#else
		1581	/* emulation, only works for normals and subnormals and +0 */
		1582	int neg = x >> 63;
		1583	int e = (x >> 52) & 0x7ffU;
		1584
		1585	x &= 0xfffffffffffffU;
		1586
		1587	if (e)
		1588	x |= 0x10000000000000U;
		1589	else
		1590	e = 1;
		1591
		1592	/* we distrust ldexp a bit and do the 2**-53 scaling by an extra multiply */
		1593	r = ldexp (x * (0.5 / 0x10000000000000U), e - 1022);
		1594
		1595	r = neg ? -r : r;
		1596	#endif
		1597
		1598	return r;
		1599	}
		1600
		1601	/* convert a float to ieee half/binary16 */
		1602	ecb_function_ ecb_const uint16_t ecb_float_to_binary16 (float x);
		1603	ecb_function_ ecb_const uint16_t
		1604	ecb_float_to_binary16 (float x)
		1605	{
		1606	return ecb_binary32_to_binary16 (ecb_float_to_binary32 (x));
		1607	}
		1608
		1609	/* convert an ieee half/binary16 to float */
		1610	ecb_function_ ecb_const float ecb_binary16_to_float (uint16_t x);
		1611	ecb_function_ ecb_const float
		1612	ecb_binary16_to_float (uint16_t x)
		1613	{
		1614	return ecb_binary32_to_float (ecb_binary16_to_binary32 (x));
		1615	}
		1616
		1617	#endif
		1618
932	#endif	1619	#endif
933		1620
934	/* ECB.H END */	1621	/* ECB.H END */
935		1622
936	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS	1623	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS
937	/* if your architecture doesn't need memory fences, e.g. because it is	1624	/* if your architecture doesn't need memory fences, e.g. because it is
938	* single-cpu/core, or if you use libev in a project that doesn't use libev	1625	* single-cpu/core, or if you use libev in a project that doesn't use libev
939	* from multiple threads, then you can define ECB_AVOID_PTHREADS when compiling	1626	* from multiple threads, then you can define ECB_NO_THREADS when compiling
940	* libev, in which cases the memory fences become nops.	1627	* libev, in which cases the memory fences become nops.
941	* alternatively, you can remove this #error and link against libpthread,	1628	* alternatively, you can remove this #error and link against libpthread,
942	* which will then provide the memory fences.	1629	* which will then provide the memory fences.
943	*/	1630	*/
944	# error "memory fences not defined for your architecture, please report"	1631	# error "memory fences not defined for your architecture, please report"
…		…
948	# define ECB_MEMORY_FENCE do { } while (0)	1635	# define ECB_MEMORY_FENCE do { } while (0)
949	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE	1636	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE
950	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	1637	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
951	#endif	1638	#endif
952		1639
953	#define expect_false(cond) ecb_expect_false (cond)
954	#define expect_true(cond) ecb_expect_true (cond)
955	#define noinline ecb_noinline
956
957	#define inline_size ecb_inline	1640	#define inline_size ecb_inline
958		1641
959	#if EV_FEATURE_CODE	1642	#if EV_FEATURE_CODE
960	# define inline_speed ecb_inline	1643	# define inline_speed ecb_inline
961	#else	1644	#else
962	# define inline_speed static noinline	1645	# define inline_speed ecb_noinline static
963	#endif	1646	#endif
964		1647
965	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)	1648	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)
966		1649
967	#if EV_MINPRI == EV_MAXPRI	1650	#if EV_MINPRI == EV_MAXPRI
968	# define ABSPRI(w) (((W)w), 0)	1651	# define ABSPRI(w) (((W)w), 0)
969	#else	1652	#else
970	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)	1653	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)
971	#endif	1654	#endif
972		1655
973	#define EMPTY /* required for microsofts broken pseudo-c compiler */	1656	#define EMPTY /* required for microsofts broken pseudo-c compiler */
974	#define EMPTY2(a,b) /* used to suppress some warnings */
975		1657
976	typedef ev_watcher *W;	1658	typedef ev_watcher *W;
977	typedef ev_watcher_list *WL;	1659	typedef ev_watcher_list *WL;
978	typedef ev_watcher_time *WT;	1660	typedef ev_watcher_time *WT;
979		1661
…		…
1004	# include "ev_win32.c"	1686	# include "ev_win32.c"
1005	#endif	1687	#endif
1006		1688
1007	/*****************************************************************************/	1689	/*****************************************************************************/
1008		1690
		1691	#if EV_USE_LINUXAIO
		1692	# include <linux/aio_abi.h> /* probably only needed for aio_context_t */
		1693	#endif
		1694
1009	/* define a suitable floor function (only used by periodics atm) */	1695	/* define a suitable floor function (only used by periodics atm) */
1010		1696
1011	#if EV_USE_FLOOR	1697	#if EV_USE_FLOOR
1012	# include <math.h>	1698	# include <math.h>
1013	# define ev_floor(v) floor (v)	1699	# define ev_floor(v) floor (v)
1014	#else	1700	#else
1015		1701
1016	#include <float.h>	1702	#include <float.h>
1017		1703
1018	/* a floor() replacement function, should be independent of ev_tstamp type */	1704	/* a floor() replacement function, should be independent of ev_tstamp type */
		1705	ecb_noinline
1019	static ev_tstamp noinline	1706	static ev_tstamp
1020	ev_floor (ev_tstamp v)	1707	ev_floor (ev_tstamp v)
1021	{	1708	{
1022	/* the choice of shift factor is not terribly important */	1709	/* the choice of shift factor is not terribly important */
1023	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */	1710	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */
1024	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;	1711	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;
1025	#else	1712	#else
1026	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;	1713	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;
1027	#endif	1714	#endif
1028		1715
1029	/* argument too large for an unsigned long? */	1716	/* argument too large for an unsigned long? */
1030	if (expect_false (v >= shift))	1717	if (ecb_expect_false (v >= shift))
1031	{	1718	{
1032	ev_tstamp f;	1719	ev_tstamp f;
1033		1720
1034	if (v == v - 1.)	1721	if (v == v - 1.)
1035	return v; /* very large number */	1722	return v; /* very large number */
…		…
1037	f = shift * ev_floor (v * (1. / shift));	1724	f = shift * ev_floor (v * (1. / shift));
1038	return f + ev_floor (v - f);	1725	return f + ev_floor (v - f);
1039	}	1726	}
1040		1727
1041	/* special treatment for negative args? */	1728	/* special treatment for negative args? */
1042	if (expect_false (v < 0.))	1729	if (ecb_expect_false (v < 0.))
1043	{	1730	{
1044	ev_tstamp f = -ev_floor (-v);	1731	ev_tstamp f = -ev_floor (-v);
1045		1732
1046	return f - (f == v ? 0 : 1);	1733	return f - (f == v ? 0 : 1);
1047	}	1734	}
…		…
1056		1743
1057	#ifdef __linux	1744	#ifdef __linux
1058	# include <sys/utsname.h>	1745	# include <sys/utsname.h>
1059	#endif	1746	#endif
1060		1747
1061	static unsigned int noinline ecb_cold	1748	ecb_noinline ecb_cold
		1749	static unsigned int
1062	ev_linux_version (void)	1750	ev_linux_version (void)
1063	{	1751	{
1064	#ifdef __linux	1752	#ifdef __linux
1065	unsigned int v = 0;	1753	unsigned int v = 0;
1066	struct utsname buf;	1754	struct utsname buf;
…		…
1095	}	1783	}
1096		1784
1097	/*****************************************************************************/	1785	/*****************************************************************************/
1098		1786
1099	#if EV_AVOID_STDIO	1787	#if EV_AVOID_STDIO
1100	static void noinline ecb_cold	1788	ecb_noinline ecb_cold
		1789	static void
1101	ev_printerr (const char *msg)	1790	ev_printerr (const char *msg)
1102	{	1791	{
1103	write (STDERR_FILENO, msg, strlen (msg));	1792	write (STDERR_FILENO, msg, strlen (msg));
1104	}	1793	}
1105	#endif	1794	#endif
1106		1795
1107	static void (*syserr_cb)(const char *msg) EV_THROW;	1796	static void (*syserr_cb)(const char *msg) EV_NOEXCEPT;
1108		1797
1109	void ecb_cold	1798	ecb_cold
		1799	void
1110	ev_set_syserr_cb (void (*cb)(const char *msg) EV_THROW) EV_THROW	1800	ev_set_syserr_cb (void (*cb)(const char *msg) EV_NOEXCEPT) EV_NOEXCEPT
1111	{	1801	{
1112	syserr_cb = cb;	1802	syserr_cb = cb;
1113	}	1803	}
1114		1804
1115	static void noinline ecb_cold	1805	ecb_noinline ecb_cold
		1806	static void
1116	ev_syserr (const char *msg)	1807	ev_syserr (const char *msg)
1117	{	1808	{
1118	if (!msg)	1809	if (!msg)
1119	msg = "(libev) system error";	1810	msg = "(libev) system error";
1120		1811
…		…
1133	abort ();	1824	abort ();
1134	}	1825	}
1135	}	1826	}
1136		1827
1137	static void *	1828	static void *
1138	ev_realloc_emul (void *ptr, long size) EV_THROW	1829	ev_realloc_emul (void *ptr, long size) EV_NOEXCEPT
1139	{	1830	{
1140	#if __GLIBC__
1141	return realloc (ptr, size);
1142	#else
1143	/* some systems, notably openbsd and darwin, fail to properly	1831	/* some systems, notably openbsd and darwin, fail to properly
1144	* implement realloc (x, 0) (as required by both ansi c-89 and	1832	* implement realloc (x, 0) (as required by both ansi c-89 and
1145	* the single unix specification, so work around them here.	1833	* the single unix specification, so work around them here.
		1834	* recently, also (at least) fedora and debian started breaking it,
		1835	* despite documenting it otherwise.
1146	*/	1836	*/
1147		1837
1148	if (size)	1838	if (size)
1149	return realloc (ptr, size);	1839	return realloc (ptr, size);
1150		1840
1151	free (ptr);	1841	free (ptr);
1152	return 0;	1842	return 0;
1153	#endif
1154	}	1843	}
1155		1844
1156	static void *(*alloc)(void *ptr, long size) EV_THROW = ev_realloc_emul;	1845	static void *(*alloc)(void *ptr, long size) EV_NOEXCEPT = ev_realloc_emul;
1157		1846
1158	void ecb_cold	1847	ecb_cold
		1848	void
1159	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_THROW) EV_THROW	1849	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_NOEXCEPT) EV_NOEXCEPT
1160	{	1850	{
1161	alloc = cb;	1851	alloc = cb;
1162	}	1852	}
1163		1853
1164	inline_speed void *	1854	inline_speed void *
…		…
1191	typedef struct	1881	typedef struct
1192	{	1882	{
1193	WL head;	1883	WL head;
1194	unsigned char events; /* the events watched for */	1884	unsigned char events; /* the events watched for */
1195	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */	1885	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */
1196	unsigned char emask; /* the epoll backend stores the actual kernel mask in here */	1886	unsigned char emask; /* some backends store the actual kernel mask in here */
1197	unsigned char unused;	1887	unsigned char unused;
1198	#if EV_USE_EPOLL	1888	#if EV_USE_EPOLL
1199	unsigned int egen; /* generation counter to counter epoll bugs */	1889	unsigned int egen; /* generation counter to counter epoll bugs */
1200	#endif	1890	#endif
1201	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP	1891	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP
…		…
1266	static int ev_default_loop_ptr;	1956	static int ev_default_loop_ptr;
1267		1957
1268	#endif	1958	#endif
1269		1959
1270	#if EV_FEATURE_API	1960	#if EV_FEATURE_API
1271	# define EV_RELEASE_CB if (expect_false (release_cb)) release_cb (EV_A)	1961	# define EV_RELEASE_CB if (ecb_expect_false (release_cb)) release_cb (EV_A)
1272	# define EV_ACQUIRE_CB if (expect_false (acquire_cb)) acquire_cb (EV_A)	1962	# define EV_ACQUIRE_CB if (ecb_expect_false (acquire_cb)) acquire_cb (EV_A)
1273	# define EV_INVOKE_PENDING invoke_cb (EV_A)	1963	# define EV_INVOKE_PENDING invoke_cb (EV_A)
1274	#else	1964	#else
1275	# define EV_RELEASE_CB (void)0	1965	# define EV_RELEASE_CB (void)0
1276	# define EV_ACQUIRE_CB (void)0	1966	# define EV_ACQUIRE_CB (void)0
1277	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)	1967	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)
…		…
1281		1971
1282	/*****************************************************************************/	1972	/*****************************************************************************/
1283		1973
1284	#ifndef EV_HAVE_EV_TIME	1974	#ifndef EV_HAVE_EV_TIME
1285	ev_tstamp	1975	ev_tstamp
1286	ev_time (void) EV_THROW	1976	ev_time (void) EV_NOEXCEPT
1287	{	1977	{
1288	#if EV_USE_REALTIME	1978	#if EV_USE_REALTIME
1289	if (expect_true (have_realtime))	1979	if (ecb_expect_true (have_realtime))
1290	{	1980	{
1291	struct timespec ts;	1981	struct timespec ts;
1292	clock_gettime (CLOCK_REALTIME, &ts);	1982	clock_gettime (CLOCK_REALTIME, &ts);
1293	return ts.tv_sec + ts.tv_nsec * 1e-9;	1983	return ts.tv_sec + ts.tv_nsec * 1e-9;
1294	}	1984	}
…		…
1302		1992
1303	inline_size ev_tstamp	1993	inline_size ev_tstamp
1304	get_clock (void)	1994	get_clock (void)
1305	{	1995	{
1306	#if EV_USE_MONOTONIC	1996	#if EV_USE_MONOTONIC
1307	if (expect_true (have_monotonic))	1997	if (ecb_expect_true (have_monotonic))
1308	{	1998	{
1309	struct timespec ts;	1999	struct timespec ts;
1310	clock_gettime (CLOCK_MONOTONIC, &ts);	2000	clock_gettime (CLOCK_MONOTONIC, &ts);
1311	return ts.tv_sec + ts.tv_nsec * 1e-9;	2001	return ts.tv_sec + ts.tv_nsec * 1e-9;
1312	}	2002	}
…		…
1315	return ev_time ();	2005	return ev_time ();
1316	}	2006	}
1317		2007
1318	#if EV_MULTIPLICITY	2008	#if EV_MULTIPLICITY
1319	ev_tstamp	2009	ev_tstamp
1320	ev_now (EV_P) EV_THROW	2010	ev_now (EV_P) EV_NOEXCEPT
1321	{	2011	{
1322	return ev_rt_now;	2012	return ev_rt_now;
1323	}	2013	}
1324	#endif	2014	#endif
1325		2015
1326	void	2016	void
1327	ev_sleep (ev_tstamp delay) EV_THROW	2017	ev_sleep (ev_tstamp delay) EV_NOEXCEPT
1328	{	2018	{
1329	if (delay > 0.)	2019	if (delay > 0.)
1330	{	2020	{
1331	#if EV_USE_NANOSLEEP	2021	#if EV_USE_NANOSLEEP
1332	struct timespec ts;	2022	struct timespec ts;
1333		2023
1334	EV_TS_SET (ts, delay);	2024	EV_TS_SET (ts, delay);
1335	nanosleep (&ts, 0);	2025	nanosleep (&ts, 0);
1336	#elif defined _WIN32	2026	#elif defined _WIN32
		2027	/* maybe this should round up, as ms is very low resolution */
		2028	/* compared to select (µs) or nanosleep (ns) */
1337	Sleep ((unsigned long)(delay * 1e3));	2029	Sleep ((unsigned long)(delay * 1e3));
1338	#else	2030	#else
1339	struct timeval tv;	2031	struct timeval tv;
1340		2032
1341	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */	2033	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */
…		…
1372	}	2064	}
1373		2065
1374	return ncur;	2066	return ncur;
1375	}	2067	}
1376		2068
1377	static void * noinline ecb_cold	2069	ecb_noinline ecb_cold
		2070	static void *
1378	array_realloc (int elem, void *base, int *cur, int cnt)	2071	array_realloc (int elem, void *base, int *cur, int cnt)
1379	{	2072	{
1380	*cur = array_nextsize (elem, *cur, cnt);	2073	*cur = array_nextsize (elem, *cur, cnt);
1381	return ev_realloc (base, elem * *cur);	2074	return ev_realloc (base, elem * *cur);
1382	}	2075	}
1383		2076
		2077	#define array_needsize_noinit(base,offset,count)
		2078
1384	#define array_init_zero(base,count) \	2079	#define array_needsize_zerofill(base,offset,count) \
1385	memset ((void *)(base), 0, sizeof (*(base)) * (count))	2080	memset ((void *)(base + offset), 0, sizeof (*(base)) * (count))
1386		2081
1387	#define array_needsize(type,base,cur,cnt,init) \	2082	#define array_needsize(type,base,cur,cnt,init) \
1388	if (expect_false ((cnt) > (cur))) \	2083	if (ecb_expect_false ((cnt) > (cur))) \
1389	{ \	2084	{ \
1390	int ecb_unused ocur_ = (cur); \	2085	ecb_unused int ocur_ = (cur); \
1391	(base) = (type *)array_realloc \	2086	(base) = (type *)array_realloc \
1392	(sizeof (type), (base), &(cur), (cnt)); \	2087	(sizeof (type), (base), &(cur), (cnt)); \
1393	init ((base) + (ocur_), (cur) - ocur_); \	2088	init ((base), ocur_, ((cur) - ocur_)); \
1394	}	2089	}
1395		2090
1396	#if 0	2091	#if 0
1397	#define array_slim(type,stem) \	2092	#define array_slim(type,stem) \
1398	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \	2093	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \
…		…
1407	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0	2102	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0
1408		2103
1409	/*****************************************************************************/	2104	/*****************************************************************************/
1410		2105
1411	/* dummy callback for pending events */	2106	/* dummy callback for pending events */
1412	static void noinline	2107	ecb_noinline
		2108	static void
1413	pendingcb (EV_P_ ev_prepare *w, int revents)	2109	pendingcb (EV_P_ ev_prepare *w, int revents)
1414	{	2110	{
1415	}	2111	}
1416		2112
1417	void noinline	2113	ecb_noinline
		2114	void
1418	ev_feed_event (EV_P_ void *w, int revents) EV_THROW	2115	ev_feed_event (EV_P_ void *w, int revents) EV_NOEXCEPT
1419	{	2116	{
1420	W w_ = (W)w;	2117	W w_ = (W)w;
1421	int pri = ABSPRI (w_);	2118	int pri = ABSPRI (w_);
1422		2119
1423	if (expect_false (w_->pending))	2120	if (ecb_expect_false (w_->pending))
1424	pendings [pri][w_->pending - 1].events |= revents;	2121	pendings [pri][w_->pending - 1].events |= revents;
1425	else	2122	else
1426	{	2123	{
1427	w_->pending = ++pendingcnt [pri];	2124	w_->pending = ++pendingcnt [pri];
1428	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, EMPTY2);	2125	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, array_needsize_noinit);
1429	pendings [pri][w_->pending - 1].w = w_;	2126	pendings [pri][w_->pending - 1].w = w_;
1430	pendings [pri][w_->pending - 1].events = revents;	2127	pendings [pri][w_->pending - 1].events = revents;
1431	}	2128	}
1432		2129
1433	pendingpri = NUMPRI - 1;	2130	pendingpri = NUMPRI - 1;
1434	}	2131	}
1435		2132
1436	inline_speed void	2133	inline_speed void
1437	feed_reverse (EV_P_ W w)	2134	feed_reverse (EV_P_ W w)
1438	{	2135	{
1439	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, EMPTY2);	2136	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, array_needsize_noinit);
1440	rfeeds [rfeedcnt++] = w;	2137	rfeeds [rfeedcnt++] = w;
1441	}	2138	}
1442		2139
1443	inline_size void	2140	inline_size void
1444	feed_reverse_done (EV_P_ int revents)	2141	feed_reverse_done (EV_P_ int revents)
…		…
1479	inline_speed void	2176	inline_speed void
1480	fd_event (EV_P_ int fd, int revents)	2177	fd_event (EV_P_ int fd, int revents)
1481	{	2178	{
1482	ANFD *anfd = anfds + fd;	2179	ANFD *anfd = anfds + fd;
1483		2180
1484	if (expect_true (!anfd->reify))	2181	if (ecb_expect_true (!anfd->reify))
1485	fd_event_nocheck (EV_A_ fd, revents);	2182	fd_event_nocheck (EV_A_ fd, revents);
1486	}	2183	}
1487		2184
1488	void	2185	void
1489	ev_feed_fd_event (EV_P_ int fd, int revents) EV_THROW	2186	ev_feed_fd_event (EV_P_ int fd, int revents) EV_NOEXCEPT
1490	{	2187	{
1491	if (fd >= 0 && fd < anfdmax)	2188	if (fd >= 0 && fd < anfdmax)
1492	fd_event_nocheck (EV_A_ fd, revents);	2189	fd_event_nocheck (EV_A_ fd, revents);
1493	}	2190	}
1494		2191
…		…
1531	ev_io *w;	2228	ev_io *w;
1532		2229
1533	unsigned char o_events = anfd->events;	2230	unsigned char o_events = anfd->events;
1534	unsigned char o_reify = anfd->reify;	2231	unsigned char o_reify = anfd->reify;
1535		2232
1536	anfd->reify = 0;	2233	anfd->reify = 0;
1537		2234
1538	/*if (expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */	2235	/*if (ecb_expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */
1539	{	2236	{
1540	anfd->events = 0;	2237	anfd->events = 0;
1541		2238
1542	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)	2239	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)
1543	anfd->events |= (unsigned char)w->events;	2240	anfd->events |= (unsigned char)w->events;
…		…
1552		2249
1553	fdchangecnt = 0;	2250	fdchangecnt = 0;
1554	}	2251	}
1555		2252
1556	/* something about the given fd changed */	2253	/* something about the given fd changed */
1557	inline_size void	2254	inline_size
		2255	void
1558	fd_change (EV_P_ int fd, int flags)	2256	fd_change (EV_P_ int fd, int flags)
1559	{	2257	{
1560	unsigned char reify = anfds [fd].reify;	2258	unsigned char reify = anfds [fd].reify;
1561	anfds [fd].reify |= flags;	2259	anfds [fd].reify |= flags;
1562		2260
1563	if (expect_true (!reify))	2261	if (ecb_expect_true (!reify))
1564	{	2262	{
1565	++fdchangecnt;	2263	++fdchangecnt;
1566	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, EMPTY2);	2264	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, array_needsize_noinit);
1567	fdchanges [fdchangecnt - 1] = fd;	2265	fdchanges [fdchangecnt - 1] = fd;
1568	}	2266	}
1569	}	2267	}
1570		2268
1571	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */	2269	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */
1572	inline_speed void ecb_cold	2270	inline_speed ecb_cold void
1573	fd_kill (EV_P_ int fd)	2271	fd_kill (EV_P_ int fd)
1574	{	2272	{
1575	ev_io *w;	2273	ev_io *w;
1576		2274
1577	while ((w = (ev_io *)anfds [fd].head))	2275	while ((w = (ev_io *)anfds [fd].head))
…		…
1580	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);	2278	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);
1581	}	2279	}
1582	}	2280	}
1583		2281
1584	/* check whether the given fd is actually valid, for error recovery */	2282	/* check whether the given fd is actually valid, for error recovery */
1585	inline_size int ecb_cold	2283	inline_size ecb_cold int
1586	fd_valid (int fd)	2284	fd_valid (int fd)
1587	{	2285	{
1588	#ifdef _WIN32	2286	#ifdef _WIN32
1589	return EV_FD_TO_WIN32_HANDLE (fd) != -1;	2287	return EV_FD_TO_WIN32_HANDLE (fd) != -1;
1590	#else	2288	#else
1591	return fcntl (fd, F_GETFD) != -1;	2289	return fcntl (fd, F_GETFD) != -1;
1592	#endif	2290	#endif
1593	}	2291	}
1594		2292
1595	/* called on EBADF to verify fds */	2293	/* called on EBADF to verify fds */
1596	static void noinline ecb_cold	2294	ecb_noinline ecb_cold
		2295	static void
1597	fd_ebadf (EV_P)	2296	fd_ebadf (EV_P)
1598	{	2297	{
1599	int fd;	2298	int fd;
1600		2299
1601	for (fd = 0; fd < anfdmax; ++fd)	2300	for (fd = 0; fd < anfdmax; ++fd)
…		…
1603	if (!fd_valid (fd) && errno == EBADF)	2302	if (!fd_valid (fd) && errno == EBADF)
1604	fd_kill (EV_A_ fd);	2303	fd_kill (EV_A_ fd);
1605	}	2304	}
1606		2305
1607	/* called on ENOMEM in select/poll to kill some fds and retry */	2306	/* called on ENOMEM in select/poll to kill some fds and retry */
1608	static void noinline ecb_cold	2307	ecb_noinline ecb_cold
		2308	static void
1609	fd_enomem (EV_P)	2309	fd_enomem (EV_P)
1610	{	2310	{
1611	int fd;	2311	int fd;
1612		2312
1613	for (fd = anfdmax; fd--; )	2313	for (fd = anfdmax; fd--; )
…		…
1617	break;	2317	break;
1618	}	2318	}
1619	}	2319	}
1620		2320
1621	/* usually called after fork if backend needs to re-arm all fds from scratch */	2321	/* usually called after fork if backend needs to re-arm all fds from scratch */
1622	static void noinline	2322	ecb_noinline
		2323	static void
1623	fd_rearm_all (EV_P)	2324	fd_rearm_all (EV_P)
1624	{	2325	{
1625	int fd;	2326	int fd;
1626		2327
1627	for (fd = 0; fd < anfdmax; ++fd)	2328	for (fd = 0; fd < anfdmax; ++fd)
…		…
1680	ev_tstamp minat;	2381	ev_tstamp minat;
1681	ANHE *minpos;	2382	ANHE *minpos;
1682	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;	2383	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;
1683		2384
1684	/* find minimum child */	2385	/* find minimum child */
1685	if (expect_true (pos + DHEAP - 1 < E))	2386	if (ecb_expect_true (pos + DHEAP - 1 < E))
1686	{	2387	{
1687	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));	2388	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));
1688	if ( ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));	2389	if ( ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));
1689	if ( ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));	2390	if ( ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));
1690	if ( ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));	2391	if ( ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));
…		…
1808		2509
1809	/*****************************************************************************/	2510	/*****************************************************************************/
1810		2511
1811	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	2512	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
1812		2513
1813	static void noinline ecb_cold	2514	ecb_noinline ecb_cold
		2515	static void
1814	evpipe_init (EV_P)	2516	evpipe_init (EV_P)
1815	{	2517	{
1816	if (!ev_is_active (&pipe_w))	2518	if (!ev_is_active (&pipe_w))
1817	{	2519	{
		2520	int fds [2];
		2521
1818	# if EV_USE_EVENTFD	2522	# if EV_USE_EVENTFD
		2523	fds [0] = -1;
1819	evfd = eventfd (0, EFD_NONBLOCK | EFD_CLOEXEC);	2524	fds [1] = eventfd (0, EFD_NONBLOCK | EFD_CLOEXEC);
1820	if (evfd < 0 && errno == EINVAL)	2525	if (fds [1] < 0 && errno == EINVAL)
1821	evfd = eventfd (0, 0);	2526	fds [1] = eventfd (0, 0);
1822		2527
1823	if (evfd >= 0)	2528	if (fds [1] < 0)
1824	{
1825	evpipe [0] = -1;
1826	fd_intern (evfd); /* doing it twice doesn't hurt */
1827	ev_io_set (&pipe_w, evfd, EV_READ);
1828	}
1829	else
1830	# endif	2529	# endif
1831	{	2530	{
1832	while (pipe (evpipe))	2531	while (pipe (fds))
1833	ev_syserr ("(libev) error creating signal/async pipe");	2532	ev_syserr ("(libev) error creating signal/async pipe");
1834		2533
1835	fd_intern (evpipe [0]);	2534	fd_intern (fds [0]);
1836	fd_intern (evpipe [1]);
1837	ev_io_set (&pipe_w, evpipe [0], EV_READ);
1838	}	2535	}
1839		2536
		2537	evpipe [0] = fds [0];
		2538
		2539	if (evpipe [1] < 0)
		2540	evpipe [1] = fds [1]; /* first call, set write fd */
		2541	else
		2542	{
		2543	/* on subsequent calls, do not change evpipe [1] */
		2544	/* so that evpipe_write can always rely on its value. */
		2545	/* this branch does not do anything sensible on windows, */
		2546	/* so must not be executed on windows */
		2547
		2548	dup2 (fds [1], evpipe [1]);
		2549	close (fds [1]);
		2550	}
		2551
		2552	fd_intern (evpipe [1]);
		2553
		2554	ev_io_set (&pipe_w, evpipe [0] < 0 ? evpipe [1] : evpipe [0], EV_READ);
1840	ev_io_start (EV_A_ &pipe_w);	2555	ev_io_start (EV_A_ &pipe_w);
1841	ev_unref (EV_A); /* watcher should not keep loop alive */	2556	ev_unref (EV_A); /* watcher should not keep loop alive */
1842	}	2557	}
1843	}	2558	}
1844		2559
1845	inline_speed void	2560	inline_speed void
1846	evpipe_write (EV_P_ EV_ATOMIC_T *flag)	2561	evpipe_write (EV_P_ EV_ATOMIC_T *flag)
1847	{	2562	{
1848	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */	2563	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */
1849		2564
1850	if (expect_true (*flag))	2565	if (ecb_expect_true (*flag))
1851	return;	2566	return;
1852		2567
1853	*flag = 1;	2568	*flag = 1;
1854	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */	2569	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */
1855		2570
…		…
1865	ECB_MEMORY_FENCE_RELEASE;	2580	ECB_MEMORY_FENCE_RELEASE;
1866		2581
1867	old_errno = errno; /* save errno because write will clobber it */	2582	old_errno = errno; /* save errno because write will clobber it */
1868		2583
1869	#if EV_USE_EVENTFD	2584	#if EV_USE_EVENTFD
1870	if (evfd >= 0)	2585	if (evpipe [0] < 0)
1871	{	2586	{
1872	uint64_t counter = 1;	2587	uint64_t counter = 1;
1873	write (evfd, &counter, sizeof (uint64_t));	2588	write (evpipe [1], &counter, sizeof (uint64_t));
1874	}	2589	}
1875	else	2590	else
1876	#endif	2591	#endif
1877	{	2592	{
1878	#ifdef _WIN32	2593	#ifdef _WIN32
1879	WSABUF buf;	2594	WSABUF buf;
1880	DWORD sent;	2595	DWORD sent;
1881	buf.buf = &buf;	2596	buf.buf = (char *)&buf;
1882	buf.len = 1;	2597	buf.len = 1;
1883	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);	2598	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);
1884	#else	2599	#else
1885	write (evpipe [1], &(evpipe [1]), 1);	2600	write (evpipe [1], &(evpipe [1]), 1);
1886	#endif	2601	#endif
…		…
1898	int i;	2613	int i;
1899		2614
1900	if (revents & EV_READ)	2615	if (revents & EV_READ)
1901	{	2616	{
1902	#if EV_USE_EVENTFD	2617	#if EV_USE_EVENTFD
1903	if (evfd >= 0)	2618	if (evpipe [0] < 0)
1904	{	2619	{
1905	uint64_t counter;	2620	uint64_t counter;
1906	read (evfd, &counter, sizeof (uint64_t));	2621	read (evpipe [1], &counter, sizeof (uint64_t));
1907	}	2622	}
1908	else	2623	else
1909	#endif	2624	#endif
1910	{	2625	{
1911	char dummy[4];	2626	char dummy[4];
…		…
1932	sig_pending = 0;	2647	sig_pending = 0;
1933		2648
1934	ECB_MEMORY_FENCE;	2649	ECB_MEMORY_FENCE;
1935		2650
1936	for (i = EV_NSIG - 1; i--; )	2651	for (i = EV_NSIG - 1; i--; )
1937	if (expect_false (signals [i].pending))	2652	if (ecb_expect_false (signals [i].pending))
1938	ev_feed_signal_event (EV_A_ i + 1);	2653	ev_feed_signal_event (EV_A_ i + 1);
1939	}	2654	}
1940	#endif	2655	#endif
1941		2656
1942	#if EV_ASYNC_ENABLE	2657	#if EV_ASYNC_ENABLE
…		…
1958	}	2673	}
1959		2674
1960	/*****************************************************************************/	2675	/*****************************************************************************/
1961		2676
1962	void	2677	void
1963	ev_feed_signal (int signum) EV_THROW	2678	ev_feed_signal (int signum) EV_NOEXCEPT
1964	{	2679	{
1965	#if EV_MULTIPLICITY	2680	#if EV_MULTIPLICITY
		2681	EV_P;
		2682	ECB_MEMORY_FENCE_ACQUIRE;
1966	EV_P = signals [signum - 1].loop;	2683	EV_A = signals [signum - 1].loop;
1967		2684
1968	if (!EV_A)	2685	if (!EV_A)
1969	return;	2686	return;
1970	#endif	2687	#endif
1971		2688
1972	if (!ev_active (&pipe_w))
1973	return;
1974
1975	signals [signum - 1].pending = 1;	2689	signals [signum - 1].pending = 1;
1976	evpipe_write (EV_A_ &sig_pending);	2690	evpipe_write (EV_A_ &sig_pending);
1977	}	2691	}
1978		2692
1979	static void	2693	static void
…		…
1984	#endif	2698	#endif
1985		2699
1986	ev_feed_signal (signum);	2700	ev_feed_signal (signum);
1987	}	2701	}
1988		2702
1989	void noinline	2703	ecb_noinline
		2704	void
1990	ev_feed_signal_event (EV_P_ int signum) EV_THROW	2705	ev_feed_signal_event (EV_P_ int signum) EV_NOEXCEPT
1991	{	2706	{
1992	WL w;	2707	WL w;
1993		2708
1994	if (expect_false (signum <= 0 || signum > EV_NSIG))	2709	if (ecb_expect_false (signum <= 0 || signum >= EV_NSIG))
1995	return;	2710	return;
1996		2711
1997	--signum;	2712	--signum;
1998		2713
1999	#if EV_MULTIPLICITY	2714	#if EV_MULTIPLICITY
2000	/* it is permissible to try to feed a signal to the wrong loop */	2715	/* it is permissible to try to feed a signal to the wrong loop */
2001	/* or, likely more useful, feeding a signal nobody is waiting for */	2716	/* or, likely more useful, feeding a signal nobody is waiting for */
2002		2717
2003	if (expect_false (signals [signum].loop != EV_A))	2718	if (ecb_expect_false (signals [signum].loop != EV_A))
2004	return;	2719	return;
2005	#endif	2720	#endif
2006		2721
2007	signals [signum].pending = 0;	2722	signals [signum].pending = 0;
2008	MEMORY_FENCE_RELEASE;	2723	ECB_MEMORY_FENCE_RELEASE;
2009		2724
2010	for (w = signals [signum].head; w; w = w->next)	2725	for (w = signals [signum].head; w; w = w->next)
2011	ev_feed_event (EV_A_ (W)w, EV_SIGNAL);	2726	ev_feed_event (EV_A_ (W)w, EV_SIGNAL);
2012	}	2727	}
2013		2728
…		…
2104	# include "ev_kqueue.c"	2819	# include "ev_kqueue.c"
2105	#endif	2820	#endif
2106	#if EV_USE_EPOLL	2821	#if EV_USE_EPOLL
2107	# include "ev_epoll.c"	2822	# include "ev_epoll.c"
2108	#endif	2823	#endif
		2824	#if EV_USE_LINUXAIO
		2825	# include "ev_linuxaio.c"
		2826	#endif
		2827	#if EV_USE_IOURING
		2828	# include "ev_iouring.c"
		2829	#endif
2109	#if EV_USE_POLL	2830	#if EV_USE_POLL
2110	# include "ev_poll.c"	2831	# include "ev_poll.c"
2111	#endif	2832	#endif
2112	#if EV_USE_SELECT	2833	#if EV_USE_SELECT
2113	# include "ev_select.c"	2834	# include "ev_select.c"
2114	#endif	2835	#endif
2115		2836
2116	int ecb_cold	2837	ecb_cold int
2117	ev_version_major (void) EV_THROW	2838	ev_version_major (void) EV_NOEXCEPT
2118	{	2839	{
2119	return EV_VERSION_MAJOR;	2840	return EV_VERSION_MAJOR;
2120	}	2841	}
2121		2842
2122	int ecb_cold	2843	ecb_cold int
2123	ev_version_minor (void) EV_THROW	2844	ev_version_minor (void) EV_NOEXCEPT
2124	{	2845	{
2125	return EV_VERSION_MINOR;	2846	return EV_VERSION_MINOR;
2126	}	2847	}
2127		2848
2128	/* return true if we are running with elevated privileges and should ignore env variables */	2849	/* return true if we are running with elevated privileges and should ignore env variables */
2129	int inline_size ecb_cold	2850	inline_size ecb_cold int
2130	enable_secure (void)	2851	enable_secure (void)
2131	{	2852	{
2132	#ifdef _WIN32	2853	#ifdef _WIN32
2133	return 0;	2854	return 0;
2134	#else	2855	#else
2135	return getuid () != geteuid ()	2856	return getuid () != geteuid ()
2136	|| getgid () != getegid ();	2857	|| getgid () != getegid ();
2137	#endif	2858	#endif
2138	}	2859	}
2139		2860
2140	unsigned int ecb_cold	2861	ecb_cold
		2862	unsigned int
2141	ev_supported_backends (void) EV_THROW	2863	ev_supported_backends (void) EV_NOEXCEPT
2142	{	2864	{
2143	unsigned int flags = 0;	2865	unsigned int flags = 0;
2144		2866
2145	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;	2867	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;
2146	if (EV_USE_KQUEUE) flags |= EVBACKEND_KQUEUE;	2868	if (EV_USE_KQUEUE ) flags |= EVBACKEND_KQUEUE;
2147	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;	2869	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;
		2870	if (EV_USE_LINUXAIO) flags |= EVBACKEND_LINUXAIO;
		2871	if (EV_USE_IOURING ) flags |= EVBACKEND_IOURING;
2148	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;	2872	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;
2149	if (EV_USE_SELECT) flags |= EVBACKEND_SELECT;	2873	if (EV_USE_SELECT ) flags |= EVBACKEND_SELECT;
2150		2874
2151	return flags;	2875	return flags;
2152	}	2876	}
2153		2877
2154	unsigned int ecb_cold	2878	ecb_cold
		2879	unsigned int
2155	ev_recommended_backends (void) EV_THROW	2880	ev_recommended_backends (void) EV_NOEXCEPT
2156	{	2881	{
2157	unsigned int flags = ev_supported_backends ();	2882	unsigned int flags = ev_supported_backends ();
2158		2883
2159	#ifndef __NetBSD__	2884	#ifndef __NetBSD__
2160	/* kqueue is borked on everything but netbsd apparently */	2885	/* kqueue is borked on everything but netbsd apparently */
…		…
2168	#endif	2893	#endif
2169	#ifdef __FreeBSD__	2894	#ifdef __FreeBSD__
2170	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */	2895	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */
2171	#endif	2896	#endif
2172		2897
		2898	/* TODO: linuxaio is very experimental */
		2899	#if !EV_RECOMMEND_LINUXAIO
		2900	flags &= ~EVBACKEND_LINUXAIO;
		2901	#endif
		2902	/* TODO: linuxaio is super experimental */
		2903	#if !EV_RECOMMEND_IOURING
		2904	flags &= ~EVBACKEND_IOURING;
		2905	#endif
		2906
2173	return flags;	2907	return flags;
2174	}	2908	}
2175		2909
2176	unsigned int ecb_cold	2910	ecb_cold
		2911	unsigned int
2177	ev_embeddable_backends (void) EV_THROW	2912	ev_embeddable_backends (void) EV_NOEXCEPT
2178	{	2913	{
2179	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;	2914	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;
2180		2915
2181	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */	2916	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */
2182	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */	2917	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */
…		…
2184		2919
2185	return flags;	2920	return flags;
2186	}	2921	}
2187		2922
2188	unsigned int	2923	unsigned int
2189	ev_backend (EV_P) EV_THROW	2924	ev_backend (EV_P) EV_NOEXCEPT
2190	{	2925	{
2191	return backend;	2926	return backend;
2192	}	2927	}
2193		2928
2194	#if EV_FEATURE_API	2929	#if EV_FEATURE_API
2195	unsigned int	2930	unsigned int
2196	ev_iteration (EV_P) EV_THROW	2931	ev_iteration (EV_P) EV_NOEXCEPT
2197	{	2932	{
2198	return loop_count;	2933	return loop_count;
2199	}	2934	}
2200		2935
2201	unsigned int	2936	unsigned int
2202	ev_depth (EV_P) EV_THROW	2937	ev_depth (EV_P) EV_NOEXCEPT
2203	{	2938	{
2204	return loop_depth;	2939	return loop_depth;
2205	}	2940	}
2206		2941
2207	void	2942	void
2208	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2943	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2209	{	2944	{
2210	io_blocktime = interval;	2945	io_blocktime = interval;
2211	}	2946	}
2212		2947
2213	void	2948	void
2214	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2949	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2215	{	2950	{
2216	timeout_blocktime = interval;	2951	timeout_blocktime = interval;
2217	}	2952	}
2218		2953
2219	void	2954	void
2220	ev_set_userdata (EV_P_ void *data) EV_THROW	2955	ev_set_userdata (EV_P_ void *data) EV_NOEXCEPT
2221	{	2956	{
2222	userdata = data;	2957	userdata = data;
2223	}	2958	}
2224		2959
2225	void *	2960	void *
2226	ev_userdata (EV_P) EV_THROW	2961	ev_userdata (EV_P) EV_NOEXCEPT
2227	{	2962	{
2228	return userdata;	2963	return userdata;
2229	}	2964	}
2230		2965
2231	void	2966	void
2232	ev_set_invoke_pending_cb (EV_P_ void (*invoke_pending_cb)(EV_P)) EV_THROW	2967	ev_set_invoke_pending_cb (EV_P_ ev_loop_callback invoke_pending_cb) EV_NOEXCEPT
2233	{	2968	{
2234	invoke_cb = invoke_pending_cb;	2969	invoke_cb = invoke_pending_cb;
2235	}	2970	}
2236		2971
2237	void	2972	void
2238	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_THROW, void (*acquire)(EV_P) EV_THROW) EV_THROW	2973	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_NOEXCEPT, void (*acquire)(EV_P) EV_NOEXCEPT) EV_NOEXCEPT
2239	{	2974	{
2240	release_cb = release;	2975	release_cb = release;
2241	acquire_cb = acquire;	2976	acquire_cb = acquire;
2242	}	2977	}
2243	#endif	2978	#endif
2244		2979
2245	/* initialise a loop structure, must be zero-initialised */	2980	/* initialise a loop structure, must be zero-initialised */
2246	static void noinline ecb_cold	2981	ecb_noinline ecb_cold
		2982	static void
2247	loop_init (EV_P_ unsigned int flags) EV_THROW	2983	loop_init (EV_P_ unsigned int flags) EV_NOEXCEPT
2248	{	2984	{
2249	if (!backend)	2985	if (!backend)
2250	{	2986	{
2251	origflags = flags;	2987	origflags = flags;
2252		2988
…		…
2297	#if EV_ASYNC_ENABLE	3033	#if EV_ASYNC_ENABLE
2298	async_pending = 0;	3034	async_pending = 0;
2299	#endif	3035	#endif
2300	pipe_write_skipped = 0;	3036	pipe_write_skipped = 0;
2301	pipe_write_wanted = 0;	3037	pipe_write_wanted = 0;
		3038	evpipe [0] = -1;
		3039	evpipe [1] = -1;
2302	#if EV_USE_INOTIFY	3040	#if EV_USE_INOTIFY
2303	fs_fd = flags & EVFLAG_NOINOTIFY ? -1 : -2;	3041	fs_fd = flags & EVFLAG_NOINOTIFY ? -1 : -2;
2304	#endif	3042	#endif
2305	#if EV_USE_SIGNALFD	3043	#if EV_USE_SIGNALFD
2306	sigfd = flags & EVFLAG_SIGNALFD ? -2 : -1;	3044	sigfd = flags & EVFLAG_SIGNALFD ? -2 : -1;
…		…
2308		3046
2309	if (!(flags & EVBACKEND_MASK))	3047	if (!(flags & EVBACKEND_MASK))
2310	flags |= ev_recommended_backends ();	3048	flags |= ev_recommended_backends ();
2311		3049
2312	#if EV_USE_IOCP	3050	#if EV_USE_IOCP
2313	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);	3051	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);
2314	#endif	3052	#endif
2315	#if EV_USE_PORT	3053	#if EV_USE_PORT
2316	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);	3054	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);
2317	#endif	3055	#endif
2318	#if EV_USE_KQUEUE	3056	#if EV_USE_KQUEUE
2319	if (!backend && (flags & EVBACKEND_KQUEUE)) backend = kqueue_init (EV_A_ flags);	3057	if (!backend && (flags & EVBACKEND_KQUEUE )) backend = kqueue_init (EV_A_ flags);
		3058	#endif
		3059	#if EV_USE_IOURING
		3060	if (!backend && (flags & EVBACKEND_IOURING )) backend = iouring_init (EV_A_ flags);
		3061	#endif
		3062	#if EV_USE_LINUXAIO
		3063	if (!backend && (flags & EVBACKEND_LINUXAIO)) backend = linuxaio_init (EV_A_ flags);
2320	#endif	3064	#endif
2321	#if EV_USE_EPOLL	3065	#if EV_USE_EPOLL
2322	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);	3066	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);
2323	#endif	3067	#endif
2324	#if EV_USE_POLL	3068	#if EV_USE_POLL
2325	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);	3069	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);
2326	#endif	3070	#endif
2327	#if EV_USE_SELECT	3071	#if EV_USE_SELECT
2328	if (!backend && (flags & EVBACKEND_SELECT)) backend = select_init (EV_A_ flags);	3072	if (!backend && (flags & EVBACKEND_SELECT )) backend = select_init (EV_A_ flags);
2329	#endif	3073	#endif
2330		3074
2331	ev_prepare_init (&pending_w, pendingcb);	3075	ev_prepare_init (&pending_w, pendingcb);
2332		3076
2333	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	3077	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
…		…
2336	#endif	3080	#endif
2337	}	3081	}
2338	}	3082	}
2339		3083
2340	/* free up a loop structure */	3084	/* free up a loop structure */
2341	void ecb_cold	3085	ecb_cold
		3086	void
2342	ev_loop_destroy (EV_P)	3087	ev_loop_destroy (EV_P)
2343	{	3088	{
2344	int i;	3089	int i;
2345		3090
2346	#if EV_MULTIPLICITY	3091	#if EV_MULTIPLICITY
…		…
2349	return;	3094	return;
2350	#endif	3095	#endif
2351		3096
2352	#if EV_CLEANUP_ENABLE	3097	#if EV_CLEANUP_ENABLE
2353	/* queue cleanup watchers (and execute them) */	3098	/* queue cleanup watchers (and execute them) */
2354	if (expect_false (cleanupcnt))	3099	if (ecb_expect_false (cleanupcnt))
2355	{	3100	{
2356	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);	3101	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);
2357	EV_INVOKE_PENDING;	3102	EV_INVOKE_PENDING;
2358	}	3103	}
2359	#endif	3104	#endif
…		…
2369	if (ev_is_active (&pipe_w))	3114	if (ev_is_active (&pipe_w))
2370	{	3115	{
2371	/*ev_ref (EV_A);*/	3116	/*ev_ref (EV_A);*/
2372	/*ev_io_stop (EV_A_ &pipe_w);*/	3117	/*ev_io_stop (EV_A_ &pipe_w);*/
2373		3118
2374	#if EV_USE_EVENTFD
2375	if (evfd >= 0)
2376	close (evfd);
2377	#endif
2378
2379	if (evpipe [0] >= 0)
2380	{
2381	EV_WIN32_CLOSE_FD (evpipe [0]);	3119	if (evpipe [0] >= 0) EV_WIN32_CLOSE_FD (evpipe [0]);
2382	EV_WIN32_CLOSE_FD (evpipe [1]);	3120	if (evpipe [1] >= 0) EV_WIN32_CLOSE_FD (evpipe [1]);
2383	}
2384	}	3121	}
2385		3122
2386	#if EV_USE_SIGNALFD	3123	#if EV_USE_SIGNALFD
2387	if (ev_is_active (&sigfd_w))	3124	if (ev_is_active (&sigfd_w))
2388	close (sigfd);	3125	close (sigfd);
…		…
2395		3132
2396	if (backend_fd >= 0)	3133	if (backend_fd >= 0)
2397	close (backend_fd);	3134	close (backend_fd);
2398		3135
2399	#if EV_USE_IOCP	3136	#if EV_USE_IOCP
2400	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);	3137	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);
2401	#endif	3138	#endif
2402	#if EV_USE_PORT	3139	#if EV_USE_PORT
2403	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);	3140	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);
2404	#endif	3141	#endif
2405	#if EV_USE_KQUEUE	3142	#if EV_USE_KQUEUE
2406	if (backend == EVBACKEND_KQUEUE) kqueue_destroy (EV_A);	3143	if (backend == EVBACKEND_KQUEUE ) kqueue_destroy (EV_A);
		3144	#endif
		3145	#if EV_USE_IOURING
		3146	if (backend == EVBACKEND_IOURING ) iouring_destroy (EV_A);
		3147	#endif
		3148	#if EV_USE_LINUXAIO
		3149	if (backend == EVBACKEND_LINUXAIO) linuxaio_destroy (EV_A);
2407	#endif	3150	#endif
2408	#if EV_USE_EPOLL	3151	#if EV_USE_EPOLL
2409	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);	3152	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);
2410	#endif	3153	#endif
2411	#if EV_USE_POLL	3154	#if EV_USE_POLL
2412	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);	3155	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);
2413	#endif	3156	#endif
2414	#if EV_USE_SELECT	3157	#if EV_USE_SELECT
2415	if (backend == EVBACKEND_SELECT) select_destroy (EV_A);	3158	if (backend == EVBACKEND_SELECT ) select_destroy (EV_A);
2416	#endif	3159	#endif
2417		3160
2418	for (i = NUMPRI; i--; )	3161	for (i = NUMPRI; i--; )
2419	{	3162	{
2420	array_free (pending, [i]);	3163	array_free (pending, [i]);
…		…
2462		3205
2463	inline_size void	3206	inline_size void
2464	loop_fork (EV_P)	3207	loop_fork (EV_P)
2465	{	3208	{
2466	#if EV_USE_PORT	3209	#if EV_USE_PORT
2467	if (backend == EVBACKEND_PORT ) port_fork (EV_A);	3210	if (backend == EVBACKEND_PORT ) port_fork (EV_A);
2468	#endif	3211	#endif
2469	#if EV_USE_KQUEUE	3212	#if EV_USE_KQUEUE
2470	if (backend == EVBACKEND_KQUEUE) kqueue_fork (EV_A);	3213	if (backend == EVBACKEND_KQUEUE ) kqueue_fork (EV_A);
		3214	#endif
		3215	#if EV_USE_IOURING
		3216	if (backend == EVBACKEND_IOURING ) iouring_fork (EV_A);
		3217	#endif
		3218	#if EV_USE_LINUXAIO
		3219	if (backend == EVBACKEND_LINUXAIO) linuxaio_fork (EV_A);
2471	#endif	3220	#endif
2472	#if EV_USE_EPOLL	3221	#if EV_USE_EPOLL
2473	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);	3222	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);
2474	#endif	3223	#endif
2475	#if EV_USE_INOTIFY	3224	#if EV_USE_INOTIFY
2476	infy_fork (EV_A);	3225	infy_fork (EV_A);
2477	#endif	3226	#endif
2478		3227
		3228	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2479	if (ev_is_active (&pipe_w))	3229	if (ev_is_active (&pipe_w) && postfork != 2)
2480	{	3230	{
2481	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */	3231	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */
2482		3232
2483	ev_ref (EV_A);	3233	ev_ref (EV_A);
2484	ev_io_stop (EV_A_ &pipe_w);	3234	ev_io_stop (EV_A_ &pipe_w);
2485		3235
2486	#if EV_USE_EVENTFD
2487	if (evfd >= 0)
2488	close (evfd);
2489	#endif
2490
2491	if (evpipe [0] >= 0)	3236	if (evpipe [0] >= 0)
2492	{
2493	EV_WIN32_CLOSE_FD (evpipe [0]);	3237	EV_WIN32_CLOSE_FD (evpipe [0]);
2494	EV_WIN32_CLOSE_FD (evpipe [1]);
2495	}
2496		3238
2497	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2498	evpipe_init (EV_A);	3239	evpipe_init (EV_A);
2499	/* now iterate over everything, in case we missed something */	3240	/* iterate over everything, in case we missed something before */
2500	pipecb (EV_A_ &pipe_w, EV_READ);	3241	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);
2501	#endif
2502	}	3242	}
		3243	#endif
2503		3244
2504	postfork = 0;	3245	postfork = 0;
2505	}	3246	}
2506		3247
2507	#if EV_MULTIPLICITY	3248	#if EV_MULTIPLICITY
2508		3249
		3250	ecb_cold
2509	struct ev_loop * ecb_cold	3251	struct ev_loop *
2510	ev_loop_new (unsigned int flags) EV_THROW	3252	ev_loop_new (unsigned int flags) EV_NOEXCEPT
2511	{	3253	{
2512	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));	3254	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));
2513		3255
2514	memset (EV_A, 0, sizeof (struct ev_loop));	3256	memset (EV_A, 0, sizeof (struct ev_loop));
2515	loop_init (EV_A_ flags);	3257	loop_init (EV_A_ flags);
…		…
2522	}	3264	}
2523		3265
2524	#endif /* multiplicity */	3266	#endif /* multiplicity */
2525		3267
2526	#if EV_VERIFY	3268	#if EV_VERIFY
2527	static void noinline ecb_cold	3269	ecb_noinline ecb_cold
		3270	static void
2528	verify_watcher (EV_P_ W w)	3271	verify_watcher (EV_P_ W w)
2529	{	3272	{
2530	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));	3273	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));
2531		3274
2532	if (w->pending)	3275	if (w->pending)
2533	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));	3276	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));
2534	}	3277	}
2535		3278
2536	static void noinline ecb_cold	3279	ecb_noinline ecb_cold
		3280	static void
2537	verify_heap (EV_P_ ANHE *heap, int N)	3281	verify_heap (EV_P_ ANHE *heap, int N)
2538	{	3282	{
2539	int i;	3283	int i;
2540		3284
2541	for (i = HEAP0; i < N + HEAP0; ++i)	3285	for (i = HEAP0; i < N + HEAP0; ++i)
…		…
2546		3290
2547	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));	3291	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));
2548	}	3292	}
2549	}	3293	}
2550		3294
2551	static void noinline ecb_cold	3295	ecb_noinline ecb_cold
		3296	static void
2552	array_verify (EV_P_ W *ws, int cnt)	3297	array_verify (EV_P_ W *ws, int cnt)
2553	{	3298	{
2554	while (cnt--)	3299	while (cnt--)
2555	{	3300	{
2556	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));	3301	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));
…		…
2559	}	3304	}
2560	#endif	3305	#endif
2561		3306
2562	#if EV_FEATURE_API	3307	#if EV_FEATURE_API
2563	void ecb_cold	3308	void ecb_cold
2564	ev_verify (EV_P) EV_THROW	3309	ev_verify (EV_P) EV_NOEXCEPT
2565	{	3310	{
2566	#if EV_VERIFY	3311	#if EV_VERIFY
2567	int i;	3312	int i;
2568	WL w, w2;	3313	WL w, w2;
2569		3314
…		…
2645	#endif	3390	#endif
2646	}	3391	}
2647	#endif	3392	#endif
2648		3393
2649	#if EV_MULTIPLICITY	3394	#if EV_MULTIPLICITY
		3395	ecb_cold
2650	struct ev_loop * ecb_cold	3396	struct ev_loop *
2651	#else	3397	#else
2652	int	3398	int
2653	#endif	3399	#endif
2654	ev_default_loop (unsigned int flags) EV_THROW	3400	ev_default_loop (unsigned int flags) EV_NOEXCEPT
2655	{	3401	{
2656	if (!ev_default_loop_ptr)	3402	if (!ev_default_loop_ptr)
2657	{	3403	{
2658	#if EV_MULTIPLICITY	3404	#if EV_MULTIPLICITY
2659	EV_P = ev_default_loop_ptr = &default_loop_struct;	3405	EV_P = ev_default_loop_ptr = &default_loop_struct;
…		…
2678		3424
2679	return ev_default_loop_ptr;	3425	return ev_default_loop_ptr;
2680	}	3426	}
2681		3427
2682	void	3428	void
2683	ev_loop_fork (EV_P) EV_THROW	3429	ev_loop_fork (EV_P) EV_NOEXCEPT
2684	{	3430	{
2685	postfork = 1; /* must be in line with ev_default_fork */	3431	postfork = 1;
2686	}	3432	}
2687		3433
2688	/*****************************************************************************/	3434	/*****************************************************************************/
2689		3435
2690	void	3436	void
…		…
2692	{	3438	{
2693	EV_CB_INVOKE ((W)w, revents);	3439	EV_CB_INVOKE ((W)w, revents);
2694	}	3440	}
2695		3441
2696	unsigned int	3442	unsigned int
2697	ev_pending_count (EV_P) EV_THROW	3443	ev_pending_count (EV_P) EV_NOEXCEPT
2698	{	3444	{
2699	int pri;	3445	int pri;
2700	unsigned int count = 0;	3446	unsigned int count = 0;
2701		3447
2702	for (pri = NUMPRI; pri--; )	3448	for (pri = NUMPRI; pri--; )
2703	count += pendingcnt [pri];	3449	count += pendingcnt [pri];
2704		3450
2705	return count;	3451	return count;
2706	}	3452	}
2707		3453
2708	void noinline	3454	ecb_noinline
		3455	void
2709	ev_invoke_pending (EV_P)	3456	ev_invoke_pending (EV_P)
2710	{	3457	{
2711	for (pendingpri = NUMPRI; pendingpri--; ) /* pendingpri is modified during the loop */	3458	pendingpri = NUMPRI;
		3459
		3460	do
		3461	{
		3462	--pendingpri;
		3463
		3464	/* pendingpri possibly gets modified in the inner loop */
2712	while (pendingcnt [pendingpri])	3465	while (pendingcnt [pendingpri])
2713	{	3466	{
2714	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];	3467	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];
2715		3468
2716	p->w->pending = 0;	3469	p->w->pending = 0;
2717	EV_CB_INVOKE (p->w, p->events);	3470	EV_CB_INVOKE (p->w, p->events);
2718	EV_FREQUENT_CHECK;	3471	EV_FREQUENT_CHECK;
2719	}	3472	}
		3473	}
		3474	while (pendingpri);
2720	}	3475	}
2721		3476
2722	#if EV_IDLE_ENABLE	3477	#if EV_IDLE_ENABLE
2723	/* make idle watchers pending. this handles the "call-idle */	3478	/* make idle watchers pending. this handles the "call-idle */
2724	/* only when higher priorities are idle" logic */	3479	/* only when higher priorities are idle" logic */
2725	inline_size void	3480	inline_size void
2726	idle_reify (EV_P)	3481	idle_reify (EV_P)
2727	{	3482	{
2728	if (expect_false (idleall))	3483	if (ecb_expect_false (idleall))
2729	{	3484	{
2730	int pri;	3485	int pri;
2731		3486
2732	for (pri = NUMPRI; pri--; )	3487	for (pri = NUMPRI; pri--; )
2733	{	3488	{
…		…
2782	}	3537	}
2783	}	3538	}
2784		3539
2785	#if EV_PERIODIC_ENABLE	3540	#if EV_PERIODIC_ENABLE
2786		3541
2787	static void noinline	3542	ecb_noinline
		3543	static void
2788	periodic_recalc (EV_P_ ev_periodic *w)	3544	periodic_recalc (EV_P_ ev_periodic *w)
2789	{	3545	{
2790	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;	3546	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;
2791	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);	3547	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);
2792		3548
…		…
2794	while (at <= ev_rt_now)	3550	while (at <= ev_rt_now)
2795	{	3551	{
2796	ev_tstamp nat = at + w->interval;	3552	ev_tstamp nat = at + w->interval;
2797		3553
2798	/* when resolution fails us, we use ev_rt_now */	3554	/* when resolution fails us, we use ev_rt_now */
2799	if (expect_false (nat == at))	3555	if (ecb_expect_false (nat == at))
2800	{	3556	{
2801	at = ev_rt_now;	3557	at = ev_rt_now;
2802	break;	3558	break;
2803	}	3559	}
2804		3560
…		…
2850	}	3606	}
2851	}	3607	}
2852		3608
2853	/* simply recalculate all periodics */	3609	/* simply recalculate all periodics */
2854	/* TODO: maybe ensure that at least one event happens when jumping forward? */	3610	/* TODO: maybe ensure that at least one event happens when jumping forward? */
2855	static void noinline ecb_cold	3611	ecb_noinline ecb_cold
		3612	static void
2856	periodics_reschedule (EV_P)	3613	periodics_reschedule (EV_P)
2857	{	3614	{
2858	int i;	3615	int i;
2859		3616
2860	/* adjust periodics after time jump */	3617	/* adjust periodics after time jump */
…		…
2873	reheap (periodics, periodiccnt);	3630	reheap (periodics, periodiccnt);
2874	}	3631	}
2875	#endif	3632	#endif
2876		3633
2877	/* adjust all timers by a given offset */	3634	/* adjust all timers by a given offset */
2878	static void noinline ecb_cold	3635	ecb_noinline ecb_cold
		3636	static void
2879	timers_reschedule (EV_P_ ev_tstamp adjust)	3637	timers_reschedule (EV_P_ ev_tstamp adjust)
2880	{	3638	{
2881	int i;	3639	int i;
2882		3640
2883	for (i = 0; i < timercnt; ++i)	3641	for (i = 0; i < timercnt; ++i)
…		…
2892	/* also detect if there was a timejump, and act accordingly */	3650	/* also detect if there was a timejump, and act accordingly */
2893	inline_speed void	3651	inline_speed void
2894	time_update (EV_P_ ev_tstamp max_block)	3652	time_update (EV_P_ ev_tstamp max_block)
2895	{	3653	{
2896	#if EV_USE_MONOTONIC	3654	#if EV_USE_MONOTONIC
2897	if (expect_true (have_monotonic))	3655	if (ecb_expect_true (have_monotonic))
2898	{	3656	{
2899	int i;	3657	int i;
2900	ev_tstamp odiff = rtmn_diff;	3658	ev_tstamp odiff = rtmn_diff;
2901		3659
2902	mn_now = get_clock ();	3660	mn_now = get_clock ();
2903		3661
2904	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */	3662	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */
2905	/* interpolate in the meantime */	3663	/* interpolate in the meantime */
2906	if (expect_true (mn_now - now_floor < MIN_TIMEJUMP * .5))	3664	if (ecb_expect_true (mn_now - now_floor < MIN_TIMEJUMP * .5))
2907	{	3665	{
2908	ev_rt_now = rtmn_diff + mn_now;	3666	ev_rt_now = rtmn_diff + mn_now;
2909	return;	3667	return;
2910	}	3668	}
2911		3669
…		…
2925	ev_tstamp diff;	3683	ev_tstamp diff;
2926	rtmn_diff = ev_rt_now - mn_now;	3684	rtmn_diff = ev_rt_now - mn_now;
2927		3685
2928	diff = odiff - rtmn_diff;	3686	diff = odiff - rtmn_diff;
2929		3687
2930	if (expect_true ((diff < 0. ? -diff : diff) < MIN_TIMEJUMP))	3688	if (ecb_expect_true ((diff < 0. ? -diff : diff) < MIN_TIMEJUMP))
2931	return; /* all is well */	3689	return; /* all is well */
2932		3690
2933	ev_rt_now = ev_time ();	3691	ev_rt_now = ev_time ();
2934	mn_now = get_clock ();	3692	mn_now = get_clock ();
2935	now_floor = mn_now;	3693	now_floor = mn_now;
…		…
2944	else	3702	else
2945	#endif	3703	#endif
2946	{	3704	{
2947	ev_rt_now = ev_time ();	3705	ev_rt_now = ev_time ();
2948		3706
2949	if (expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + MIN_TIMEJUMP))	3707	if (ecb_expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + MIN_TIMEJUMP))
2950	{	3708	{
2951	/* adjust timers. this is easy, as the offset is the same for all of them */	3709	/* adjust timers. this is easy, as the offset is the same for all of them */
2952	timers_reschedule (EV_A_ ev_rt_now - mn_now);	3710	timers_reschedule (EV_A_ ev_rt_now - mn_now);
2953	#if EV_PERIODIC_ENABLE	3711	#if EV_PERIODIC_ENABLE
2954	periodics_reschedule (EV_A);	3712	periodics_reschedule (EV_A);
…		…
2977	#if EV_VERIFY >= 2	3735	#if EV_VERIFY >= 2
2978	ev_verify (EV_A);	3736	ev_verify (EV_A);
2979	#endif	3737	#endif
2980		3738
2981	#ifndef _WIN32	3739	#ifndef _WIN32
2982	if (expect_false (curpid)) /* penalise the forking check even more */	3740	if (ecb_expect_false (curpid)) /* penalise the forking check even more */
2983	if (expect_false (getpid () != curpid))	3741	if (ecb_expect_false (getpid () != curpid))
2984	{	3742	{
2985	curpid = getpid ();	3743	curpid = getpid ();
2986	postfork = 1;	3744	postfork = 1;
2987	}	3745	}
2988	#endif	3746	#endif
2989		3747
2990	#if EV_FORK_ENABLE	3748	#if EV_FORK_ENABLE
2991	/* we might have forked, so queue fork handlers */	3749	/* we might have forked, so queue fork handlers */
2992	if (expect_false (postfork))	3750	if (ecb_expect_false (postfork))
2993	if (forkcnt)	3751	if (forkcnt)
2994	{	3752	{
2995	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);	3753	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);
2996	EV_INVOKE_PENDING;	3754	EV_INVOKE_PENDING;
2997	}	3755	}
2998	#endif	3756	#endif
2999		3757
3000	#if EV_PREPARE_ENABLE	3758	#if EV_PREPARE_ENABLE
3001	/* queue prepare watchers (and execute them) */	3759	/* queue prepare watchers (and execute them) */
3002	if (expect_false (preparecnt))	3760	if (ecb_expect_false (preparecnt))
3003	{	3761	{
3004	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);	3762	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);
3005	EV_INVOKE_PENDING;	3763	EV_INVOKE_PENDING;
3006	}	3764	}
3007	#endif	3765	#endif
3008		3766
3009	if (expect_false (loop_done))	3767	if (ecb_expect_false (loop_done))
3010	break;	3768	break;
3011		3769
3012	/* we might have forked, so reify kernel state if necessary */	3770	/* we might have forked, so reify kernel state if necessary */
3013	if (expect_false (postfork))	3771	if (ecb_expect_false (postfork))
3014	loop_fork (EV_A);	3772	loop_fork (EV_A);
3015		3773
3016	/* update fd-related kernel structures */	3774	/* update fd-related kernel structures */
3017	fd_reify (EV_A);	3775	fd_reify (EV_A);
3018		3776
…		…
3030	/* from now on, we want a pipe-wake-up */	3788	/* from now on, we want a pipe-wake-up */
3031	pipe_write_wanted = 1;	3789	pipe_write_wanted = 1;
3032		3790
3033	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */	3791	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */
3034		3792
3035	if (expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))	3793	if (ecb_expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))
3036	{	3794	{
3037	waittime = MAX_BLOCKTIME;	3795	waittime = MAX_BLOCKTIME;
3038		3796
3039	if (timercnt)	3797	if (timercnt)
3040	{	3798	{
…		…
3049	if (waittime > to) waittime = to;	3807	if (waittime > to) waittime = to;
3050	}	3808	}
3051	#endif	3809	#endif
3052		3810
3053	/* don't let timeouts decrease the waittime below timeout_blocktime */	3811	/* don't let timeouts decrease the waittime below timeout_blocktime */
3054	if (expect_false (waittime < timeout_blocktime))	3812	if (ecb_expect_false (waittime < timeout_blocktime))
3055	waittime = timeout_blocktime;	3813	waittime = timeout_blocktime;
3056		3814
3057	/* at this point, we NEED to wait, so we have to ensure */	3815	/* at this point, we NEED to wait, so we have to ensure */
3058	/* to pass a minimum nonzero value to the backend */	3816	/* to pass a minimum nonzero value to the backend */
3059	if (expect_false (waittime < backend_mintime))	3817	if (ecb_expect_false (waittime < backend_mintime))
3060	waittime = backend_mintime;	3818	waittime = backend_mintime;
3061		3819
3062	/* extra check because io_blocktime is commonly 0 */	3820	/* extra check because io_blocktime is commonly 0 */
3063	if (expect_false (io_blocktime))	3821	if (ecb_expect_false (io_blocktime))
3064	{	3822	{
3065	sleeptime = io_blocktime - (mn_now - prev_mn_now);	3823	sleeptime = io_blocktime - (mn_now - prev_mn_now);
3066		3824
3067	if (sleeptime > waittime - backend_mintime)	3825	if (sleeptime > waittime - backend_mintime)
3068	sleeptime = waittime - backend_mintime;	3826	sleeptime = waittime - backend_mintime;
3069		3827
3070	if (expect_true (sleeptime > 0.))	3828	if (ecb_expect_true (sleeptime > 0.))
3071	{	3829	{
3072	ev_sleep (sleeptime);	3830	ev_sleep (sleeptime);
3073	waittime -= sleeptime;	3831	waittime -= sleeptime;
3074	}	3832	}
3075	}	3833	}
…		…
3082	backend_poll (EV_A_ waittime);	3840	backend_poll (EV_A_ waittime);
3083	assert ((loop_done = EVBREAK_CANCEL, 1)); /* assert for side effect */	3841	assert ((loop_done = EVBREAK_CANCEL, 1)); /* assert for side effect */
3084		3842
3085	pipe_write_wanted = 0; /* just an optimisation, no fence needed */	3843	pipe_write_wanted = 0; /* just an optimisation, no fence needed */
3086		3844
		3845	ECB_MEMORY_FENCE_ACQUIRE;
3087	if (pipe_write_skipped)	3846	if (pipe_write_skipped)
3088	{	3847	{
3089	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));	3848	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));
3090	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);	3849	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);
3091	}	3850	}
3092		3851
3093
3094	/* update ev_rt_now, do magic */	3852	/* update ev_rt_now, do magic */
3095	time_update (EV_A_ waittime + sleeptime);	3853	time_update (EV_A_ waittime + sleeptime);
3096	}	3854	}
3097		3855
3098	/* queue pending timers and reschedule them */	3856	/* queue pending timers and reschedule them */
…		…
3106	idle_reify (EV_A);	3864	idle_reify (EV_A);
3107	#endif	3865	#endif
3108		3866
3109	#if EV_CHECK_ENABLE	3867	#if EV_CHECK_ENABLE
3110	/* queue check watchers, to be executed first */	3868	/* queue check watchers, to be executed first */
3111	if (expect_false (checkcnt))	3869	if (ecb_expect_false (checkcnt))
3112	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);	3870	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);
3113	#endif	3871	#endif
3114		3872
3115	EV_INVOKE_PENDING;	3873	EV_INVOKE_PENDING;
3116	}	3874	}
3117	while (expect_true (	3875	while (ecb_expect_true (
3118	activecnt	3876	activecnt
3119	&& !loop_done	3877	&& !loop_done
3120	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))	3878	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))
3121	));	3879	));
3122		3880
…		…
3129		3887
3130	return activecnt;	3888	return activecnt;
3131	}	3889	}
3132		3890
3133	void	3891	void
3134	ev_break (EV_P_ int how) EV_THROW	3892	ev_break (EV_P_ int how) EV_NOEXCEPT
3135	{	3893	{
3136	loop_done = how;	3894	loop_done = how;
3137	}	3895	}
3138		3896
3139	void	3897	void
3140	ev_ref (EV_P) EV_THROW	3898	ev_ref (EV_P) EV_NOEXCEPT
3141	{	3899	{
3142	++activecnt;	3900	++activecnt;
3143	}	3901	}
3144		3902
3145	void	3903	void
3146	ev_unref (EV_P) EV_THROW	3904	ev_unref (EV_P) EV_NOEXCEPT
3147	{	3905	{
3148	--activecnt;	3906	--activecnt;
3149	}	3907	}
3150		3908
3151	void	3909	void
3152	ev_now_update (EV_P) EV_THROW	3910	ev_now_update (EV_P) EV_NOEXCEPT
3153	{	3911	{
3154	time_update (EV_A_ 1e100);	3912	time_update (EV_A_ 1e100);
3155	}	3913	}
3156		3914
3157	void	3915	void
3158	ev_suspend (EV_P) EV_THROW	3916	ev_suspend (EV_P) EV_NOEXCEPT
3159	{	3917	{
3160	ev_now_update (EV_A);	3918	ev_now_update (EV_A);
3161	}	3919	}
3162		3920
3163	void	3921	void
3164	ev_resume (EV_P) EV_THROW	3922	ev_resume (EV_P) EV_NOEXCEPT
3165	{	3923	{
3166	ev_tstamp mn_prev = mn_now;	3924	ev_tstamp mn_prev = mn_now;
3167		3925
3168	ev_now_update (EV_A);	3926	ev_now_update (EV_A);
3169	timers_reschedule (EV_A_ mn_now - mn_prev);	3927	timers_reschedule (EV_A_ mn_now - mn_prev);
…		…
3186	inline_size void	3944	inline_size void
3187	wlist_del (WL *head, WL elem)	3945	wlist_del (WL *head, WL elem)
3188	{	3946	{
3189	while (*head)	3947	while (*head)
3190	{	3948	{
3191	if (expect_true (*head == elem))	3949	if (ecb_expect_true (*head == elem))
3192	{	3950	{
3193	*head = elem->next;	3951	*head = elem->next;
3194	break;	3952	break;
3195	}	3953	}
3196		3954
…		…
3208	w->pending = 0;	3966	w->pending = 0;
3209	}	3967	}
3210	}	3968	}
3211		3969
3212	int	3970	int
3213	ev_clear_pending (EV_P_ void *w) EV_THROW	3971	ev_clear_pending (EV_P_ void *w) EV_NOEXCEPT
3214	{	3972	{
3215	W w_ = (W)w;	3973	W w_ = (W)w;
3216	int pending = w_->pending;	3974	int pending = w_->pending;
3217		3975
3218	if (expect_true (pending))	3976	if (ecb_expect_true (pending))
3219	{	3977	{
3220	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;	3978	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;
3221	p->w = (W)&pending_w;	3979	p->w = (W)&pending_w;
3222	w_->pending = 0;	3980	w_->pending = 0;
3223	return p->events;	3981	return p->events;
…		…
3250	w->active = 0;	4008	w->active = 0;
3251	}	4009	}
3252		4010
3253	/*****************************************************************************/	4011	/*****************************************************************************/
3254		4012
3255	void noinline	4013	ecb_noinline
		4014	void
3256	ev_io_start (EV_P_ ev_io *w) EV_THROW	4015	ev_io_start (EV_P_ ev_io *w) EV_NOEXCEPT
3257	{	4016	{
3258	int fd = w->fd;	4017	int fd = w->fd;
3259		4018
3260	if (expect_false (ev_is_active (w)))	4019	if (ecb_expect_false (ev_is_active (w)))
3261	return;	4020	return;
3262		4021
3263	assert (("libev: ev_io_start called with negative fd", fd >= 0));	4022	assert (("libev: ev_io_start called with negative fd", fd >= 0));
3264	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));	4023	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));
3265		4024
		4025	#if EV_VERIFY >= 2
		4026	assert (("libev: ev_io_start called on watcher with invalid fd", fd_valid (fd)));
		4027	#endif
3266	EV_FREQUENT_CHECK;	4028	EV_FREQUENT_CHECK;
3267		4029
3268	ev_start (EV_A_ (W)w, 1);	4030	ev_start (EV_A_ (W)w, 1);
3269	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_init_zero);	4031	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_needsize_zerofill);
3270	wlist_add (&anfds[fd].head, (WL)w);	4032	wlist_add (&anfds[fd].head, (WL)w);
3271		4033
3272	/* common bug, apparently */	4034	/* common bug, apparently */
3273	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));	4035	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));
3274		4036
…		…
3276	w->events &= ~EV__IOFDSET;	4038	w->events &= ~EV__IOFDSET;
3277		4039
3278	EV_FREQUENT_CHECK;	4040	EV_FREQUENT_CHECK;
3279	}	4041	}
3280		4042
3281	void noinline	4043	ecb_noinline
		4044	void
3282	ev_io_stop (EV_P_ ev_io *w) EV_THROW	4045	ev_io_stop (EV_P_ ev_io *w) EV_NOEXCEPT
3283	{	4046	{
3284	clear_pending (EV_A_ (W)w);	4047	clear_pending (EV_A_ (W)w);
3285	if (expect_false (!ev_is_active (w)))	4048	if (ecb_expect_false (!ev_is_active (w)))
3286	return;	4049	return;
3287		4050
3288	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));	4051	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));
3289		4052
		4053	#if EV_VERIFY >= 2
		4054	assert (("libev: ev_io_stop called on watcher with invalid fd", fd_valid (w->fd)));
		4055	#endif
3290	EV_FREQUENT_CHECK;	4056	EV_FREQUENT_CHECK;
3291		4057
3292	wlist_del (&anfds[w->fd].head, (WL)w);	4058	wlist_del (&anfds[w->fd].head, (WL)w);
3293	ev_stop (EV_A_ (W)w);	4059	ev_stop (EV_A_ (W)w);
3294		4060
3295	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);	4061	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);
3296		4062
3297	EV_FREQUENT_CHECK;	4063	EV_FREQUENT_CHECK;
3298	}	4064	}
3299		4065
3300	void noinline	4066	ecb_noinline
		4067	void
3301	ev_timer_start (EV_P_ ev_timer *w) EV_THROW	4068	ev_timer_start (EV_P_ ev_timer *w) EV_NOEXCEPT
3302	{	4069	{
3303	if (expect_false (ev_is_active (w)))	4070	if (ecb_expect_false (ev_is_active (w)))
3304	return;	4071	return;
3305		4072
3306	ev_at (w) += mn_now;	4073	ev_at (w) += mn_now;
3307		4074
3308	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));	4075	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));
3309		4076
3310	EV_FREQUENT_CHECK;	4077	EV_FREQUENT_CHECK;
3311		4078
3312	++timercnt;	4079	++timercnt;
3313	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);	4080	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);
3314	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, EMPTY2);	4081	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, array_needsize_noinit);
3315	ANHE_w (timers [ev_active (w)]) = (WT)w;	4082	ANHE_w (timers [ev_active (w)]) = (WT)w;
3316	ANHE_at_cache (timers [ev_active (w)]);	4083	ANHE_at_cache (timers [ev_active (w)]);
3317	upheap (timers, ev_active (w));	4084	upheap (timers, ev_active (w));
3318		4085
3319	EV_FREQUENT_CHECK;	4086	EV_FREQUENT_CHECK;
3320		4087
3321	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/	4088	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/
3322	}	4089	}
3323		4090
3324	void noinline	4091	ecb_noinline
		4092	void
3325	ev_timer_stop (EV_P_ ev_timer *w) EV_THROW	4093	ev_timer_stop (EV_P_ ev_timer *w) EV_NOEXCEPT
3326	{	4094	{
3327	clear_pending (EV_A_ (W)w);	4095	clear_pending (EV_A_ (W)w);
3328	if (expect_false (!ev_is_active (w)))	4096	if (ecb_expect_false (!ev_is_active (w)))
3329	return;	4097	return;
3330		4098
3331	EV_FREQUENT_CHECK;	4099	EV_FREQUENT_CHECK;
3332		4100
3333	{	4101	{
…		…
3335		4103
3336	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));	4104	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));
3337		4105
3338	--timercnt;	4106	--timercnt;
3339		4107
3340	if (expect_true (active < timercnt + HEAP0))	4108	if (ecb_expect_true (active < timercnt + HEAP0))
3341	{	4109	{
3342	timers [active] = timers [timercnt + HEAP0];	4110	timers [active] = timers [timercnt + HEAP0];
3343	adjustheap (timers, timercnt, active);	4111	adjustheap (timers, timercnt, active);
3344	}	4112	}
3345	}	4113	}
…		…
3349	ev_stop (EV_A_ (W)w);	4117	ev_stop (EV_A_ (W)w);
3350		4118
3351	EV_FREQUENT_CHECK;	4119	EV_FREQUENT_CHECK;
3352	}	4120	}
3353		4121
3354	void noinline	4122	ecb_noinline
		4123	void
3355	ev_timer_again (EV_P_ ev_timer *w) EV_THROW	4124	ev_timer_again (EV_P_ ev_timer *w) EV_NOEXCEPT
3356	{	4125	{
3357	EV_FREQUENT_CHECK;	4126	EV_FREQUENT_CHECK;
3358		4127
3359	clear_pending (EV_A_ (W)w);	4128	clear_pending (EV_A_ (W)w);
3360		4129
…		…
3377		4146
3378	EV_FREQUENT_CHECK;	4147	EV_FREQUENT_CHECK;
3379	}	4148	}
3380		4149
3381	ev_tstamp	4150	ev_tstamp
3382	ev_timer_remaining (EV_P_ ev_timer *w) EV_THROW	4151	ev_timer_remaining (EV_P_ ev_timer *w) EV_NOEXCEPT
3383	{	4152	{
3384	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);	4153	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);
3385	}	4154	}
3386		4155
3387	#if EV_PERIODIC_ENABLE	4156	#if EV_PERIODIC_ENABLE
3388	void noinline	4157	ecb_noinline
		4158	void
3389	ev_periodic_start (EV_P_ ev_periodic *w) EV_THROW	4159	ev_periodic_start (EV_P_ ev_periodic *w) EV_NOEXCEPT
3390	{	4160	{
3391	if (expect_false (ev_is_active (w)))	4161	if (ecb_expect_false (ev_is_active (w)))
3392	return;	4162	return;
3393		4163
3394	if (w->reschedule_cb)	4164	if (w->reschedule_cb)
3395	ev_at (w) = w->reschedule_cb (w, ev_rt_now);	4165	ev_at (w) = w->reschedule_cb (w, ev_rt_now);
3396	else if (w->interval)	4166	else if (w->interval)
…		…
3403		4173
3404	EV_FREQUENT_CHECK;	4174	EV_FREQUENT_CHECK;
3405		4175
3406	++periodiccnt;	4176	++periodiccnt;
3407	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);	4177	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);
3408	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, EMPTY2);	4178	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, array_needsize_noinit);
3409	ANHE_w (periodics [ev_active (w)]) = (WT)w;	4179	ANHE_w (periodics [ev_active (w)]) = (WT)w;
3410	ANHE_at_cache (periodics [ev_active (w)]);	4180	ANHE_at_cache (periodics [ev_active (w)]);
3411	upheap (periodics, ev_active (w));	4181	upheap (periodics, ev_active (w));
3412		4182
3413	EV_FREQUENT_CHECK;	4183	EV_FREQUENT_CHECK;
3414		4184
3415	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/	4185	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/
3416	}	4186	}
3417		4187
3418	void noinline	4188	ecb_noinline
		4189	void
3419	ev_periodic_stop (EV_P_ ev_periodic *w) EV_THROW	4190	ev_periodic_stop (EV_P_ ev_periodic *w) EV_NOEXCEPT
3420	{	4191	{
3421	clear_pending (EV_A_ (W)w);	4192	clear_pending (EV_A_ (W)w);
3422	if (expect_false (!ev_is_active (w)))	4193	if (ecb_expect_false (!ev_is_active (w)))
3423	return;	4194	return;
3424		4195
3425	EV_FREQUENT_CHECK;	4196	EV_FREQUENT_CHECK;
3426		4197
3427	{	4198	{
…		…
3429		4200
3430	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));	4201	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));
3431		4202
3432	--periodiccnt;	4203	--periodiccnt;
3433		4204
3434	if (expect_true (active < periodiccnt + HEAP0))	4205	if (ecb_expect_true (active < periodiccnt + HEAP0))
3435	{	4206	{
3436	periodics [active] = periodics [periodiccnt + HEAP0];	4207	periodics [active] = periodics [periodiccnt + HEAP0];
3437	adjustheap (periodics, periodiccnt, active);	4208	adjustheap (periodics, periodiccnt, active);
3438	}	4209	}
3439	}	4210	}
…		…
3441	ev_stop (EV_A_ (W)w);	4212	ev_stop (EV_A_ (W)w);
3442		4213
3443	EV_FREQUENT_CHECK;	4214	EV_FREQUENT_CHECK;
3444	}	4215	}
3445		4216
3446	void noinline	4217	ecb_noinline
		4218	void
3447	ev_periodic_again (EV_P_ ev_periodic *w) EV_THROW	4219	ev_periodic_again (EV_P_ ev_periodic *w) EV_NOEXCEPT
3448	{	4220	{
3449	/* TODO: use adjustheap and recalculation */	4221	/* TODO: use adjustheap and recalculation */
3450	ev_periodic_stop (EV_A_ w);	4222	ev_periodic_stop (EV_A_ w);
3451	ev_periodic_start (EV_A_ w);	4223	ev_periodic_start (EV_A_ w);
3452	}	4224	}
…		…
3456	# define SA_RESTART 0	4228	# define SA_RESTART 0
3457	#endif	4229	#endif
3458		4230
3459	#if EV_SIGNAL_ENABLE	4231	#if EV_SIGNAL_ENABLE
3460		4232
3461	void noinline	4233	ecb_noinline
		4234	void
3462	ev_signal_start (EV_P_ ev_signal *w) EV_THROW	4235	ev_signal_start (EV_P_ ev_signal *w) EV_NOEXCEPT
3463	{	4236	{
3464	if (expect_false (ev_is_active (w)))	4237	if (ecb_expect_false (ev_is_active (w)))
3465	return;	4238	return;
3466		4239
3467	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));	4240	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));
3468		4241
3469	#if EV_MULTIPLICITY	4242	#if EV_MULTIPLICITY
3470	assert (("libev: a signal must not be attached to two different loops",	4243	assert (("libev: a signal must not be attached to two different loops",
3471	!signals [w->signum - 1].loop || signals [w->signum - 1].loop == loop));	4244	!signals [w->signum - 1].loop || signals [w->signum - 1].loop == loop));
3472		4245
3473	signals [w->signum - 1].loop = EV_A;	4246	signals [w->signum - 1].loop = EV_A;
		4247	ECB_MEMORY_FENCE_RELEASE;
3474	#endif	4248	#endif
3475		4249
3476	EV_FREQUENT_CHECK;	4250	EV_FREQUENT_CHECK;
3477		4251
3478	#if EV_USE_SIGNALFD	4252	#if EV_USE_SIGNALFD
…		…
3537	}	4311	}
3538		4312
3539	EV_FREQUENT_CHECK;	4313	EV_FREQUENT_CHECK;
3540	}	4314	}
3541		4315
3542	void noinline	4316	ecb_noinline
		4317	void
3543	ev_signal_stop (EV_P_ ev_signal *w) EV_THROW	4318	ev_signal_stop (EV_P_ ev_signal *w) EV_NOEXCEPT
3544	{	4319	{
3545	clear_pending (EV_A_ (W)w);	4320	clear_pending (EV_A_ (W)w);
3546	if (expect_false (!ev_is_active (w)))	4321	if (ecb_expect_false (!ev_is_active (w)))
3547	return;	4322	return;
3548		4323
3549	EV_FREQUENT_CHECK;	4324	EV_FREQUENT_CHECK;
3550		4325
3551	wlist_del (&signals [w->signum - 1].head, (WL)w);	4326	wlist_del (&signals [w->signum - 1].head, (WL)w);
…		…
3579	#endif	4354	#endif
3580		4355
3581	#if EV_CHILD_ENABLE	4356	#if EV_CHILD_ENABLE
3582		4357
3583	void	4358	void
3584	ev_child_start (EV_P_ ev_child *w) EV_THROW	4359	ev_child_start (EV_P_ ev_child *w) EV_NOEXCEPT
3585	{	4360	{
3586	#if EV_MULTIPLICITY	4361	#if EV_MULTIPLICITY
3587	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));	4362	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));
3588	#endif	4363	#endif
3589	if (expect_false (ev_is_active (w)))	4364	if (ecb_expect_false (ev_is_active (w)))
3590	return;	4365	return;
3591		4366
3592	EV_FREQUENT_CHECK;	4367	EV_FREQUENT_CHECK;
3593		4368
3594	ev_start (EV_A_ (W)w, 1);	4369	ev_start (EV_A_ (W)w, 1);
…		…
3596		4371
3597	EV_FREQUENT_CHECK;	4372	EV_FREQUENT_CHECK;
3598	}	4373	}
3599		4374
3600	void	4375	void
3601	ev_child_stop (EV_P_ ev_child *w) EV_THROW	4376	ev_child_stop (EV_P_ ev_child *w) EV_NOEXCEPT
3602	{	4377	{
3603	clear_pending (EV_A_ (W)w);	4378	clear_pending (EV_A_ (W)w);
3604	if (expect_false (!ev_is_active (w)))	4379	if (ecb_expect_false (!ev_is_active (w)))
3605	return;	4380	return;
3606		4381
3607	EV_FREQUENT_CHECK;	4382	EV_FREQUENT_CHECK;
3608		4383
3609	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);	4384	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);
…		…
3623		4398
3624	#define DEF_STAT_INTERVAL 5.0074891	4399	#define DEF_STAT_INTERVAL 5.0074891
3625	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */	4400	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */
3626	#define MIN_STAT_INTERVAL 0.1074891	4401	#define MIN_STAT_INTERVAL 0.1074891
3627		4402
3628	static void noinline stat_timer_cb (EV_P_ ev_timer *w_, int revents);	4403	ecb_noinline static void stat_timer_cb (EV_P_ ev_timer *w_, int revents);
3629		4404
3630	#if EV_USE_INOTIFY	4405	#if EV_USE_INOTIFY
3631		4406
3632	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */	4407	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */
3633	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)	4408	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)
3634		4409
3635	static void noinline	4410	ecb_noinline
		4411	static void
3636	infy_add (EV_P_ ev_stat *w)	4412	infy_add (EV_P_ ev_stat *w)
3637	{	4413	{
3638	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);	4414	w->wd = inotify_add_watch (fs_fd, w->path,
		4415	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY
		4416	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO
		4417	| IN_DONT_FOLLOW | IN_MASK_ADD);
3639		4418
3640	if (w->wd >= 0)	4419	if (w->wd >= 0)
3641	{	4420	{
3642	struct statfs sfs;	4421	struct statfs sfs;
3643		4422
…		…
3647		4426
3648	if (!fs_2625)	4427	if (!fs_2625)
3649	w->timer.repeat = w->interval ? w->interval : DEF_STAT_INTERVAL;	4428	w->timer.repeat = w->interval ? w->interval : DEF_STAT_INTERVAL;
3650	else if (!statfs (w->path, &sfs)	4429	else if (!statfs (w->path, &sfs)
3651	&& (sfs.f_type == 0x1373 /* devfs */	4430	&& (sfs.f_type == 0x1373 /* devfs */
		4431	|| sfs.f_type == 0x4006 /* fat */
		4432	|| sfs.f_type == 0x4d44 /* msdos */
3652	|| sfs.f_type == 0xEF53 /* ext2/3 */	4433	|| sfs.f_type == 0xEF53 /* ext2/3 */
		4434	|| sfs.f_type == 0x72b6 /* jffs2 */
		4435	|| sfs.f_type == 0x858458f6 /* ramfs */
		4436	|| sfs.f_type == 0x5346544e /* ntfs */
3653	|| sfs.f_type == 0x3153464a /* jfs */	4437	|| sfs.f_type == 0x3153464a /* jfs */
		4438	|| sfs.f_type == 0x9123683e /* btrfs */
3654	|| sfs.f_type == 0x52654973 /* reiser3 */	4439	|| sfs.f_type == 0x52654973 /* reiser3 */
3655	|| sfs.f_type == 0x01021994 /* tempfs */	4440	|| sfs.f_type == 0x01021994 /* tmpfs */
3656	|| sfs.f_type == 0x58465342 /* xfs */))	4441	|| sfs.f_type == 0x58465342 /* xfs */))
3657	w->timer.repeat = 0.; /* filesystem is local, kernel new enough */	4442	w->timer.repeat = 0.; /* filesystem is local, kernel new enough */
3658	else	4443	else
3659	w->timer.repeat = w->interval ? w->interval : NFS_STAT_INTERVAL; /* remote, use reduced frequency */	4444	w->timer.repeat = w->interval ? w->interval : NFS_STAT_INTERVAL; /* remote, use reduced frequency */
3660	}	4445	}
…		…
3695	if (ev_is_active (&w->timer)) ev_ref (EV_A);	4480	if (ev_is_active (&w->timer)) ev_ref (EV_A);
3696	ev_timer_again (EV_A_ &w->timer);	4481	ev_timer_again (EV_A_ &w->timer);
3697	if (ev_is_active (&w->timer)) ev_unref (EV_A);	4482	if (ev_is_active (&w->timer)) ev_unref (EV_A);
3698	}	4483	}
3699		4484
3700	static void noinline	4485	ecb_noinline
		4486	static void
3701	infy_del (EV_P_ ev_stat *w)	4487	infy_del (EV_P_ ev_stat *w)
3702	{	4488	{
3703	int slot;	4489	int slot;
3704	int wd = w->wd;	4490	int wd = w->wd;
3705		4491
…		…
3712		4498
3713	/* remove this watcher, if others are watching it, they will rearm */	4499	/* remove this watcher, if others are watching it, they will rearm */
3714	inotify_rm_watch (fs_fd, wd);	4500	inotify_rm_watch (fs_fd, wd);
3715	}	4501	}
3716		4502
3717	static void noinline	4503	ecb_noinline
		4504	static void
3718	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)	4505	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)
3719	{	4506	{
3720	if (slot < 0)	4507	if (slot < 0)
3721	/* overflow, need to check for all hash slots */	4508	/* overflow, need to check for all hash slots */
3722	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)	4509	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)
…		…
3758	infy_wd (EV_A_ ev->wd, ev->wd, ev);	4545	infy_wd (EV_A_ ev->wd, ev->wd, ev);
3759	ofs += sizeof (struct inotify_event) + ev->len;	4546	ofs += sizeof (struct inotify_event) + ev->len;
3760	}	4547	}
3761	}	4548	}
3762		4549
3763	inline_size void ecb_cold	4550	inline_size ecb_cold
		4551	void
3764	ev_check_2625 (EV_P)	4552	ev_check_2625 (EV_P)
3765	{	4553	{
3766	/* kernels < 2.6.25 are borked	4554	/* kernels < 2.6.25 are borked
3767	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html	4555	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html
3768	*/	4556	*/
…		…
3858	#else	4646	#else
3859	# define EV_LSTAT(p,b) lstat (p, b)	4647	# define EV_LSTAT(p,b) lstat (p, b)
3860	#endif	4648	#endif
3861		4649
3862	void	4650	void
3863	ev_stat_stat (EV_P_ ev_stat *w) EV_THROW	4651	ev_stat_stat (EV_P_ ev_stat *w) EV_NOEXCEPT
3864	{	4652	{
3865	if (lstat (w->path, &w->attr) < 0)	4653	if (lstat (w->path, &w->attr) < 0)
3866	w->attr.st_nlink = 0;	4654	w->attr.st_nlink = 0;
3867	else if (!w->attr.st_nlink)	4655	else if (!w->attr.st_nlink)
3868	w->attr.st_nlink = 1;	4656	w->attr.st_nlink = 1;
3869	}	4657	}
3870		4658
3871	static void noinline	4659	ecb_noinline
		4660	static void
3872	stat_timer_cb (EV_P_ ev_timer *w_, int revents)	4661	stat_timer_cb (EV_P_ ev_timer *w_, int revents)
3873	{	4662	{
3874	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));	4663	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));
3875		4664
3876	ev_statdata prev = w->attr;	4665	ev_statdata prev = w->attr;
…		…
3907	ev_feed_event (EV_A_ w, EV_STAT);	4696	ev_feed_event (EV_A_ w, EV_STAT);
3908	}	4697	}
3909	}	4698	}
3910		4699
3911	void	4700	void
3912	ev_stat_start (EV_P_ ev_stat *w) EV_THROW	4701	ev_stat_start (EV_P_ ev_stat *w) EV_NOEXCEPT
3913	{	4702	{
3914	if (expect_false (ev_is_active (w)))	4703	if (ecb_expect_false (ev_is_active (w)))
3915	return;	4704	return;
3916		4705
3917	ev_stat_stat (EV_A_ w);	4706	ev_stat_stat (EV_A_ w);
3918		4707
3919	if (w->interval < MIN_STAT_INTERVAL && w->interval)	4708	if (w->interval < MIN_STAT_INTERVAL && w->interval)
…		…
3938		4727
3939	EV_FREQUENT_CHECK;	4728	EV_FREQUENT_CHECK;
3940	}	4729	}
3941		4730
3942	void	4731	void
3943	ev_stat_stop (EV_P_ ev_stat *w) EV_THROW	4732	ev_stat_stop (EV_P_ ev_stat *w) EV_NOEXCEPT
3944	{	4733	{
3945	clear_pending (EV_A_ (W)w);	4734	clear_pending (EV_A_ (W)w);
3946	if (expect_false (!ev_is_active (w)))	4735	if (ecb_expect_false (!ev_is_active (w)))
3947	return;	4736	return;
3948		4737
3949	EV_FREQUENT_CHECK;	4738	EV_FREQUENT_CHECK;
3950		4739
3951	#if EV_USE_INOTIFY	4740	#if EV_USE_INOTIFY
…		…
3964	}	4753	}
3965	#endif	4754	#endif
3966		4755
3967	#if EV_IDLE_ENABLE	4756	#if EV_IDLE_ENABLE
3968	void	4757	void
3969	ev_idle_start (EV_P_ ev_idle *w) EV_THROW	4758	ev_idle_start (EV_P_ ev_idle *w) EV_NOEXCEPT
3970	{	4759	{
3971	if (expect_false (ev_is_active (w)))	4760	if (ecb_expect_false (ev_is_active (w)))
3972	return;	4761	return;
3973		4762
3974	pri_adjust (EV_A_ (W)w);	4763	pri_adjust (EV_A_ (W)w);
3975		4764
3976	EV_FREQUENT_CHECK;	4765	EV_FREQUENT_CHECK;
…		…
3979	int active = ++idlecnt [ABSPRI (w)];	4768	int active = ++idlecnt [ABSPRI (w)];
3980		4769
3981	++idleall;	4770	++idleall;
3982	ev_start (EV_A_ (W)w, active);	4771	ev_start (EV_A_ (W)w, active);
3983		4772
3984	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, EMPTY2);	4773	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, array_needsize_noinit);
3985	idles [ABSPRI (w)][active - 1] = w;	4774	idles [ABSPRI (w)][active - 1] = w;
3986	}	4775	}
3987		4776
3988	EV_FREQUENT_CHECK;	4777	EV_FREQUENT_CHECK;
3989	}	4778	}
3990		4779
3991	void	4780	void
3992	ev_idle_stop (EV_P_ ev_idle *w) EV_THROW	4781	ev_idle_stop (EV_P_ ev_idle *w) EV_NOEXCEPT
3993	{	4782	{
3994	clear_pending (EV_A_ (W)w);	4783	clear_pending (EV_A_ (W)w);
3995	if (expect_false (!ev_is_active (w)))	4784	if (ecb_expect_false (!ev_is_active (w)))
3996	return;	4785	return;
3997		4786
3998	EV_FREQUENT_CHECK;	4787	EV_FREQUENT_CHECK;
3999		4788
4000	{	4789	{
…		…
4011	}	4800	}
4012	#endif	4801	#endif
4013		4802
4014	#if EV_PREPARE_ENABLE	4803	#if EV_PREPARE_ENABLE
4015	void	4804	void
4016	ev_prepare_start (EV_P_ ev_prepare *w) EV_THROW	4805	ev_prepare_start (EV_P_ ev_prepare *w) EV_NOEXCEPT
4017	{	4806	{
4018	if (expect_false (ev_is_active (w)))	4807	if (ecb_expect_false (ev_is_active (w)))
4019	return;	4808	return;
4020		4809
4021	EV_FREQUENT_CHECK;	4810	EV_FREQUENT_CHECK;
4022		4811
4023	ev_start (EV_A_ (W)w, ++preparecnt);	4812	ev_start (EV_A_ (W)w, ++preparecnt);
4024	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, EMPTY2);	4813	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, array_needsize_noinit);
4025	prepares [preparecnt - 1] = w;	4814	prepares [preparecnt - 1] = w;
4026		4815
4027	EV_FREQUENT_CHECK;	4816	EV_FREQUENT_CHECK;
4028	}	4817	}
4029		4818
4030	void	4819	void
4031	ev_prepare_stop (EV_P_ ev_prepare *w) EV_THROW	4820	ev_prepare_stop (EV_P_ ev_prepare *w) EV_NOEXCEPT
4032	{	4821	{
4033	clear_pending (EV_A_ (W)w);	4822	clear_pending (EV_A_ (W)w);
4034	if (expect_false (!ev_is_active (w)))	4823	if (ecb_expect_false (!ev_is_active (w)))
4035	return;	4824	return;
4036		4825
4037	EV_FREQUENT_CHECK;	4826	EV_FREQUENT_CHECK;
4038		4827
4039	{	4828	{
…		…
4049	}	4838	}
4050	#endif	4839	#endif
4051		4840
4052	#if EV_CHECK_ENABLE	4841	#if EV_CHECK_ENABLE
4053	void	4842	void
4054	ev_check_start (EV_P_ ev_check *w) EV_THROW	4843	ev_check_start (EV_P_ ev_check *w) EV_NOEXCEPT
4055	{	4844	{
4056	if (expect_false (ev_is_active (w)))	4845	if (ecb_expect_false (ev_is_active (w)))
4057	return;	4846	return;
4058		4847
4059	EV_FREQUENT_CHECK;	4848	EV_FREQUENT_CHECK;
4060		4849
4061	ev_start (EV_A_ (W)w, ++checkcnt);	4850	ev_start (EV_A_ (W)w, ++checkcnt);
4062	array_needsize (ev_check *, checks, checkmax, checkcnt, EMPTY2);	4851	array_needsize (ev_check *, checks, checkmax, checkcnt, array_needsize_noinit);
4063	checks [checkcnt - 1] = w;	4852	checks [checkcnt - 1] = w;
4064		4853
4065	EV_FREQUENT_CHECK;	4854	EV_FREQUENT_CHECK;
4066	}	4855	}
4067		4856
4068	void	4857	void
4069	ev_check_stop (EV_P_ ev_check *w) EV_THROW	4858	ev_check_stop (EV_P_ ev_check *w) EV_NOEXCEPT
4070	{	4859	{
4071	clear_pending (EV_A_ (W)w);	4860	clear_pending (EV_A_ (W)w);
4072	if (expect_false (!ev_is_active (w)))	4861	if (ecb_expect_false (!ev_is_active (w)))
4073	return;	4862	return;
4074		4863
4075	EV_FREQUENT_CHECK;	4864	EV_FREQUENT_CHECK;
4076		4865
4077	{	4866	{
…		…
4086	EV_FREQUENT_CHECK;	4875	EV_FREQUENT_CHECK;
4087	}	4876	}
4088	#endif	4877	#endif
4089		4878
4090	#if EV_EMBED_ENABLE	4879	#if EV_EMBED_ENABLE
4091	void noinline	4880	ecb_noinline
		4881	void
4092	ev_embed_sweep (EV_P_ ev_embed *w) EV_THROW	4882	ev_embed_sweep (EV_P_ ev_embed *w) EV_NOEXCEPT
4093	{	4883	{
4094	ev_run (w->other, EVRUN_NOWAIT);	4884	ev_run (w->other, EVRUN_NOWAIT);
4095	}	4885	}
4096		4886
4097	static void	4887	static void
…		…
4145	ev_idle_stop (EV_A_ idle);	4935	ev_idle_stop (EV_A_ idle);
4146	}	4936	}
4147	#endif	4937	#endif
4148		4938
4149	void	4939	void
4150	ev_embed_start (EV_P_ ev_embed *w) EV_THROW	4940	ev_embed_start (EV_P_ ev_embed *w) EV_NOEXCEPT
4151	{	4941	{
4152	if (expect_false (ev_is_active (w)))	4942	if (ecb_expect_false (ev_is_active (w)))
4153	return;	4943	return;
4154		4944
4155	{	4945	{
4156	EV_P = w->other;	4946	EV_P = w->other;
4157	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));	4947	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));
…		…
4176		4966
4177	EV_FREQUENT_CHECK;	4967	EV_FREQUENT_CHECK;
4178	}	4968	}
4179		4969
4180	void	4970	void
4181	ev_embed_stop (EV_P_ ev_embed *w) EV_THROW	4971	ev_embed_stop (EV_P_ ev_embed *w) EV_NOEXCEPT
4182	{	4972	{
4183	clear_pending (EV_A_ (W)w);	4973	clear_pending (EV_A_ (W)w);
4184	if (expect_false (!ev_is_active (w)))	4974	if (ecb_expect_false (!ev_is_active (w)))
4185	return;	4975	return;
4186		4976
4187	EV_FREQUENT_CHECK;	4977	EV_FREQUENT_CHECK;
4188		4978
4189	ev_io_stop (EV_A_ &w->io);	4979	ev_io_stop (EV_A_ &w->io);
…		…
4196	}	4986	}
4197	#endif	4987	#endif
4198		4988
4199	#if EV_FORK_ENABLE	4989	#if EV_FORK_ENABLE
4200	void	4990	void
4201	ev_fork_start (EV_P_ ev_fork *w) EV_THROW	4991	ev_fork_start (EV_P_ ev_fork *w) EV_NOEXCEPT
4202	{	4992	{
4203	if (expect_false (ev_is_active (w)))	4993	if (ecb_expect_false (ev_is_active (w)))
4204	return;	4994	return;
4205		4995
4206	EV_FREQUENT_CHECK;	4996	EV_FREQUENT_CHECK;
4207		4997
4208	ev_start (EV_A_ (W)w, ++forkcnt);	4998	ev_start (EV_A_ (W)w, ++forkcnt);
4209	array_needsize (ev_fork *, forks, forkmax, forkcnt, EMPTY2);	4999	array_needsize (ev_fork *, forks, forkmax, forkcnt, array_needsize_noinit);
4210	forks [forkcnt - 1] = w;	5000	forks [forkcnt - 1] = w;
4211		5001
4212	EV_FREQUENT_CHECK;	5002	EV_FREQUENT_CHECK;
4213	}	5003	}
4214		5004
4215	void	5005	void
4216	ev_fork_stop (EV_P_ ev_fork *w) EV_THROW	5006	ev_fork_stop (EV_P_ ev_fork *w) EV_NOEXCEPT
4217	{	5007	{
4218	clear_pending (EV_A_ (W)w);	5008	clear_pending (EV_A_ (W)w);
4219	if (expect_false (!ev_is_active (w)))	5009	if (ecb_expect_false (!ev_is_active (w)))
4220	return;	5010	return;
4221		5011
4222	EV_FREQUENT_CHECK;	5012	EV_FREQUENT_CHECK;
4223		5013
4224	{	5014	{
…		…
4234	}	5024	}
4235	#endif	5025	#endif
4236		5026
4237	#if EV_CLEANUP_ENABLE	5027	#if EV_CLEANUP_ENABLE
4238	void	5028	void
4239	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_THROW	5029	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4240	{	5030	{
4241	if (expect_false (ev_is_active (w)))	5031	if (ecb_expect_false (ev_is_active (w)))
4242	return;	5032	return;
4243		5033
4244	EV_FREQUENT_CHECK;	5034	EV_FREQUENT_CHECK;
4245		5035
4246	ev_start (EV_A_ (W)w, ++cleanupcnt);	5036	ev_start (EV_A_ (W)w, ++cleanupcnt);
4247	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, EMPTY2);	5037	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, array_needsize_noinit);
4248	cleanups [cleanupcnt - 1] = w;	5038	cleanups [cleanupcnt - 1] = w;
4249		5039
4250	/* cleanup watchers should never keep a refcount on the loop */	5040	/* cleanup watchers should never keep a refcount on the loop */
4251	ev_unref (EV_A);	5041	ev_unref (EV_A);
4252	EV_FREQUENT_CHECK;	5042	EV_FREQUENT_CHECK;
4253	}	5043	}
4254		5044
4255	void	5045	void
4256	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_THROW	5046	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4257	{	5047	{
4258	clear_pending (EV_A_ (W)w);	5048	clear_pending (EV_A_ (W)w);
4259	if (expect_false (!ev_is_active (w)))	5049	if (ecb_expect_false (!ev_is_active (w)))
4260	return;	5050	return;
4261		5051
4262	EV_FREQUENT_CHECK;	5052	EV_FREQUENT_CHECK;
4263	ev_ref (EV_A);	5053	ev_ref (EV_A);
4264		5054
…		…
4275	}	5065	}
4276	#endif	5066	#endif
4277		5067
4278	#if EV_ASYNC_ENABLE	5068	#if EV_ASYNC_ENABLE
4279	void	5069	void
4280	ev_async_start (EV_P_ ev_async *w) EV_THROW	5070	ev_async_start (EV_P_ ev_async *w) EV_NOEXCEPT
4281	{	5071	{
4282	if (expect_false (ev_is_active (w)))	5072	if (ecb_expect_false (ev_is_active (w)))
4283	return;	5073	return;
4284		5074
4285	w->sent = 0;	5075	w->sent = 0;
4286		5076
4287	evpipe_init (EV_A);	5077	evpipe_init (EV_A);
4288		5078
4289	EV_FREQUENT_CHECK;	5079	EV_FREQUENT_CHECK;
4290		5080
4291	ev_start (EV_A_ (W)w, ++asynccnt);	5081	ev_start (EV_A_ (W)w, ++asynccnt);
4292	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, EMPTY2);	5082	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, array_needsize_noinit);
4293	asyncs [asynccnt - 1] = w;	5083	asyncs [asynccnt - 1] = w;
4294		5084
4295	EV_FREQUENT_CHECK;	5085	EV_FREQUENT_CHECK;
4296	}	5086	}
4297		5087
4298	void	5088	void
4299	ev_async_stop (EV_P_ ev_async *w) EV_THROW	5089	ev_async_stop (EV_P_ ev_async *w) EV_NOEXCEPT
4300	{	5090	{
4301	clear_pending (EV_A_ (W)w);	5091	clear_pending (EV_A_ (W)w);
4302	if (expect_false (!ev_is_active (w)))	5092	if (ecb_expect_false (!ev_is_active (w)))
4303	return;	5093	return;
4304		5094
4305	EV_FREQUENT_CHECK;	5095	EV_FREQUENT_CHECK;
4306		5096
4307	{	5097	{
…		…
4315		5105
4316	EV_FREQUENT_CHECK;	5106	EV_FREQUENT_CHECK;
4317	}	5107	}
4318		5108
4319	void	5109	void
4320	ev_async_send (EV_P_ ev_async *w) EV_THROW	5110	ev_async_send (EV_P_ ev_async *w) EV_NOEXCEPT
4321	{	5111	{
4322	w->sent = 1;	5112	w->sent = 1;
4323	evpipe_write (EV_A_ &async_pending);	5113	evpipe_write (EV_A_ &async_pending);
4324	}	5114	}
4325	#endif	5115	#endif
…		…
4362		5152
4363	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));	5153	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));
4364	}	5154	}
4365		5155
4366	void	5156	void
4367	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_THROW	5157	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_NOEXCEPT
4368	{	5158	{
4369	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));	5159	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));
4370
4371	if (expect_false (!once))
4372	{
4373	cb (EV_ERROR | EV_READ | EV_WRITE | EV_TIMER, arg);
4374	return;
4375	}
4376		5160
4377	once->cb = cb;	5161	once->cb = cb;
4378	once->arg = arg;	5162	once->arg = arg;
4379		5163
4380	ev_init (&once->io, once_cb_io);	5164	ev_init (&once->io, once_cb_io);
…		…
4393	}	5177	}
4394		5178
4395	/*****************************************************************************/	5179	/*****************************************************************************/
4396		5180
4397	#if EV_WALK_ENABLE	5181	#if EV_WALK_ENABLE
4398	void ecb_cold	5182	ecb_cold
		5183	void
4399	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_THROW	5184	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_NOEXCEPT
4400	{	5185	{
4401	int i, j;	5186	int i, j;
4402	ev_watcher_list *wl, *wn;	5187	ev_watcher_list *wl, *wn;
4403		5188
4404	if (types & (EV_IO | EV_EMBED))	5189	if (types & (EV_IO | EV_EMBED))

Diff Legend

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