ViewVC Help

View File | Revision Log | Show Annotations | Download File

/cvs/libev/ev.c

Comparing libev/ev.c (file contents):
Revision 1.460 by root, Tue Oct 29 12:53:38 2013 UTC vs.
Revision 1.514 by root, Fri Dec 20 05:20:50 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
…		…
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	118	# endif
119		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
		127	# endif
		128
		129	# if HAVE_LINUX_FS_H && HAVE_SYS_TIMERFD_H && HAVE_KERNEL_RWF_T
		130	# ifndef EV_USE_IOURING
		131	# define EV_USE_IOURING EV_FEATURE_BACKENDS
		132	# endif
		133	# else
		134	# undef EV_USE_IOURING
		135	# define EV_USE_IOURING 0
		136	# endif
		137
120	# if HAVE_KQUEUE && HAVE_SYS_EVENT_H	138	# if HAVE_KQUEUE && HAVE_SYS_EVENT_H
121	# ifndef EV_USE_KQUEUE	139	# ifndef EV_USE_KQUEUE
122	# define EV_USE_KQUEUE EV_FEATURE_BACKENDS	140	# define EV_USE_KQUEUE EV_FEATURE_BACKENDS
123	# endif	141	# endif
124	# else	142	# else
…		…
159	# endif	177	# endif
160	# else	178	# else
161	# undef EV_USE_EVENTFD	179	# undef EV_USE_EVENTFD
162	# define EV_USE_EVENTFD 0	180	# define EV_USE_EVENTFD 0
163	# endif	181	# endif
164		182
165	#endif	183	#endif
		184
		185	/* OS X, in its infinite idiocy, actually HARDCODES
		186	* a limit of 1024 into their select. Where people have brains,
		187	* OS X engineers apparently have a vacuum. Or maybe they were
		188	* ordered to have a vacuum, or they do anything for money.
		189	* This might help. Or not.
		190	* Note that this must be defined early, as other include files
		191	* will rely on this define as well.
		192	*/
		193	#define _DARWIN_UNLIMITED_SELECT 1
166		194
167	#include <stdlib.h>	195	#include <stdlib.h>
168	#include <string.h>	196	#include <string.h>
169	#include <fcntl.h>	197	#include <fcntl.h>
170	#include <stddef.h>	198	#include <stddef.h>
…		…
208	# ifndef EV_SELECT_IS_WINSOCKET	236	# ifndef EV_SELECT_IS_WINSOCKET
209	# define EV_SELECT_IS_WINSOCKET 1	237	# define EV_SELECT_IS_WINSOCKET 1
210	# endif	238	# endif
211	# undef EV_AVOID_STDIO	239	# undef EV_AVOID_STDIO
212	#endif	240	#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		241
222	/* this block tries to deduce configuration from header-defined symbols and defaults */	242	/* this block tries to deduce configuration from header-defined symbols and defaults */
223		243
224	/* try to deduce the maximum number of signals on this platform */	244	/* try to deduce the maximum number of signals on this platform */
225	#if defined EV_NSIG	245	#if defined EV_NSIG
…		…
256	# else	276	# else
257	# define EV_USE_CLOCK_SYSCALL 0	277	# define EV_USE_CLOCK_SYSCALL 0
258	# endif	278	# endif
259	#endif	279	#endif
260		280
		281	#if !(_POSIX_TIMERS > 0)
		282	# ifndef EV_USE_MONOTONIC
		283	# define EV_USE_MONOTONIC 0
		284	# endif
		285	# ifndef EV_USE_REALTIME
		286	# define EV_USE_REALTIME 0
		287	# endif
		288	#endif
		289
261	#ifndef EV_USE_MONOTONIC	290	#ifndef EV_USE_MONOTONIC
262	# if defined _POSIX_MONOTONIC_CLOCK && _POSIX_MONOTONIC_CLOCK >= 0	291	# if defined _POSIX_MONOTONIC_CLOCK && _POSIX_MONOTONIC_CLOCK >= 0
263	# define EV_USE_MONOTONIC EV_FEATURE_OS	292	# define EV_USE_MONOTONIC EV_FEATURE_OS
264	# else	293	# else
265	# define EV_USE_MONOTONIC 0	294	# define EV_USE_MONOTONIC 0
…		…
304		333
305	#ifndef EV_USE_PORT	334	#ifndef EV_USE_PORT
306	# define EV_USE_PORT 0	335	# define EV_USE_PORT 0
307	#endif	336	#endif
308		337
		338	#ifndef EV_USE_LINUXAIO
		339	# if __linux /* libev currently assumes linux/aio_abi.h is always available on linux */
		340	# define EV_USE_LINUXAIO 1
		341	# else
		342	# define EV_USE_LINUXAIO 0
		343	# endif
		344	#endif
		345
		346	#ifndef EV_USE_IOURING
		347	# if __linux /* later checks might disable again */
		348	# define EV_USE_IOURING 1
		349	# else
		350	# define EV_USE_IOURING 0
		351	# endif
		352	#endif
		353
309	#ifndef EV_USE_INOTIFY	354	#ifndef EV_USE_INOTIFY
310	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))	355	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))
311	# define EV_USE_INOTIFY EV_FEATURE_OS	356	# define EV_USE_INOTIFY EV_FEATURE_OS
312	# else	357	# else
313	# define EV_USE_INOTIFY 0	358	# define EV_USE_INOTIFY 0
…		…
354		399
355	#ifndef EV_HEAP_CACHE_AT	400	#ifndef EV_HEAP_CACHE_AT
356	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA	401	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA
357	#endif	402	#endif
358		403
359	#ifdef ANDROID	404	#ifdef __ANDROID__
360	/* supposedly, android doesn't typedef fd_mask */	405	/* supposedly, android doesn't typedef fd_mask */
361	# undef EV_USE_SELECT	406	# undef EV_USE_SELECT
362	# define EV_USE_SELECT 0	407	# define EV_USE_SELECT 0
363	/* supposedly, we need to include syscall.h, not sys/syscall.h, so just disable */	408	/* supposedly, we need to include syscall.h, not sys/syscall.h, so just disable */
364	# undef EV_USE_CLOCK_SYSCALL	409	# undef EV_USE_CLOCK_SYSCALL
…		…
378	# include <sys/syscall.h>	423	# include <sys/syscall.h>
379	# ifdef SYS_clock_gettime	424	# ifdef SYS_clock_gettime
380	# define clock_gettime(id, ts) syscall (SYS_clock_gettime, (id), (ts))	425	# define clock_gettime(id, ts) syscall (SYS_clock_gettime, (id), (ts))
381	# undef EV_USE_MONOTONIC	426	# undef EV_USE_MONOTONIC
382	# define EV_USE_MONOTONIC 1	427	# define EV_USE_MONOTONIC 1
		428	# define EV_NEED_SYSCALL 1
383	# else	429	# else
384	# undef EV_USE_CLOCK_SYSCALL	430	# undef EV_USE_CLOCK_SYSCALL
385	# define EV_USE_CLOCK_SYSCALL 0	431	# define EV_USE_CLOCK_SYSCALL 0
386	# endif	432	# endif
387	#endif	433	#endif
…		…
401	#if !EV_STAT_ENABLE	447	#if !EV_STAT_ENABLE
402	# undef EV_USE_INOTIFY	448	# undef EV_USE_INOTIFY
403	# define EV_USE_INOTIFY 0	449	# define EV_USE_INOTIFY 0
404	#endif	450	#endif
405		451
		452	#if __linux && EV_USE_IOURING
		453	# include <linux/version.h>
		454	# if LINUX_VERSION_CODE < KERNEL_VERSION(4,14,0)
		455	# undef EV_USE_IOURING
		456	# define EV_USE_IOURING 0
		457	# endif
		458	#endif
		459
406	#if !EV_USE_NANOSLEEP	460	#if !EV_USE_NANOSLEEP
407	/* hp-ux has it in sys/time.h, which we unconditionally include above */	461	/* hp-ux has it in sys/time.h, which we unconditionally include above */
408	# if !defined _WIN32 && !defined __hpux	462	# if !defined _WIN32 && !defined __hpux
409	# include <sys/select.h>	463	# include <sys/select.h>
		464	# endif
		465	#endif
		466
		467	#if EV_USE_LINUXAIO
		468	# include <sys/syscall.h>
		469	# if SYS_io_getevents && EV_USE_EPOLL /* linuxaio backend requires epoll backend */
		470	# define EV_NEED_SYSCALL 1
		471	# else
		472	# undef EV_USE_LINUXAIO
		473	# define EV_USE_LINUXAIO 0
		474	# endif
		475	#endif
		476
		477	#if EV_USE_IOURING
		478	# include <sys/syscall.h>
		479	# if !SYS_io_uring_setup && __linux && !__alpha
		480	# define SYS_io_uring_setup 425
		481	# define SYS_io_uring_enter 426
		482	# define SYS_io_uring_wregister 427
		483	# endif
		484	# if SYS_io_uring_setup && EV_USE_EPOLL /* iouring backend requires epoll backend */
		485	# define EV_NEED_SYSCALL 1
		486	# else
		487	# undef EV_USE_IOURING
		488	# define EV_USE_IOURING 0
410	# endif	489	# endif
411	#endif	490	#endif
412		491
413	#if EV_USE_INOTIFY	492	#if EV_USE_INOTIFY
414	# include <sys/statfs.h>	493	# include <sys/statfs.h>
…		…
456	uint32_t ssi_signo;	535	uint32_t ssi_signo;
457	char pad[128 - sizeof (uint32_t)];	536	char pad[128 - sizeof (uint32_t)];
458	};	537	};
459	#endif	538	#endif
460		539
461	/**/	540	/*****************************************************************************/
462		541
463	#if EV_VERIFY >= 3	542	#if EV_VERIFY >= 3
464	# define EV_FREQUENT_CHECK ev_verify (EV_A)	543	# define EV_FREQUENT_CHECK ev_verify (EV_A)
465	#else	544	#else
466	# define EV_FREQUENT_CHECK do { } while (0)	545	# define EV_FREQUENT_CHECK do { } while (0)
…		…
471	* This value is good at least till the year 4000.	550	* This value is good at least till the year 4000.
472	*/	551	*/
473	#define MIN_INTERVAL 0.0001220703125 /* 1/2**13, good till 4000 */	552	#define MIN_INTERVAL 0.0001220703125 /* 1/2**13, good till 4000 */
474	/*#define MIN_INTERVAL 0.00000095367431640625 /* 1/2**20, good till 2200 */	553	/*#define MIN_INTERVAL 0.00000095367431640625 /* 1/2**20, good till 2200 */
475		554
476	#define MIN_TIMEJUMP 1. /* minimum timejump that gets detected (if monotonic clock available) */	555	#define MIN_TIMEJUMP 1. /* minimum timejump that gets detected (if monotonic clock available) */
477	#define MAX_BLOCKTIME 59.743 /* never wait longer than this time (to detect time jumps) */	556	#define MAX_BLOCKTIME 59.743 /* never wait longer than this time (to detect time jumps) */
478		557
		558	/* find a portable timestamp that is "always" in the future but fits into time_t.
		559	* this is quite hard, and we are mostly guessing - we handle 32 bit signed/unsigned time_t,
		560	* and sizes larger than 32 bit, and maybe the unlikely floating point time_t */
		561	#define EV_TSTAMP_HUGE \
		562	(sizeof (time_t) >= 8 ? 10000000000000. \
		563	: 0 < (time_t)4294967295 ? 4294967295. \
		564	: 2147483647.) \
		565
		566	#ifndef EV_TS_CONST
		567	# define EV_TS_CONST(nv) nv
		568	# define EV_TS_TO_MSEC(a) a * 1e3 + 0.9999
		569	# define EV_TS_FROM_USEC(us) us * 1e-6
479	#define EV_TV_SET(tv,t) do { tv.tv_sec = (long)t; tv.tv_usec = (long)((t - tv.tv_sec) * 1e6); } while (0)	570	# define EV_TV_SET(tv,t) do { tv.tv_sec = (long)t; tv.tv_usec = (long)((t - tv.tv_sec) * 1e6); } while (0)
480	#define EV_TS_SET(ts,t) do { ts.tv_sec = (long)t; ts.tv_nsec = (long)((t - ts.tv_sec) * 1e9); } while (0)	571	# define EV_TS_SET(ts,t) do { ts.tv_sec = (long)t; ts.tv_nsec = (long)((t - ts.tv_sec) * 1e9); } while (0)
		572	# define EV_TV_GET(tv) ((tv).tv_sec + (tv).tv_usec * 1e-6)
		573	# define EV_TS_GET(ts) ((ts).tv_sec + (ts).tv_nsec * 1e-9)
		574	#endif
481		575
482	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */	576	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */
483	/* ECB.H BEGIN */	577	/* ECB.H BEGIN */
484	/*	578	/*
485	* libecb - http://software.schmorp.de/pkg/libecb	579	* libecb - http://software.schmorp.de/pkg/libecb
486	*	580	*
487	* Copyright (©) 2009-2012 Marc Alexander Lehmann <libecb@schmorp.de>	581	* Copyright (©) 2009-2015 Marc Alexander Lehmann <libecb@schmorp.de>
488	* Copyright (©) 2011 Emanuele Giaquinta	582	* Copyright (©) 2011 Emanuele Giaquinta
489	* All rights reserved.	583	* All rights reserved.
490	*	584	*
491	* Redistribution and use in source and binary forms, with or without modifica-	585	* Redistribution and use in source and binary forms, with or without modifica-
492	* tion, are permitted provided that the following conditions are met:	586	* tion, are permitted provided that the following conditions are met:
…		…
506	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;	600	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;
507	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,	601	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,
508	* WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING NEGLIGENCE OR OTH-	602	* WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING NEGLIGENCE OR OTH-
509	* ERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED	603	* ERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED
510	* OF THE POSSIBILITY OF SUCH DAMAGE.	604	* OF THE POSSIBILITY OF SUCH DAMAGE.
		605	*
		606	* Alternatively, the contents of this file may be used under the terms of
		607	* the GNU General Public License ("GPL") version 2 or any later version,
		608	* in which case the provisions of the GPL are applicable instead of
		609	* the above. If you wish to allow the use of your version of this file
		610	* only under the terms of the GPL and not to allow others to use your
		611	* version of this file under the BSD license, indicate your decision
		612	* by deleting the provisions above and replace them with the notice
		613	* and other provisions required by the GPL. If you do not delete the
		614	* provisions above, a recipient may use your version of this file under
		615	* either the BSD or the GPL.
511	*/	616	*/
512		617
513	#ifndef ECB_H	618	#ifndef ECB_H
514	#define ECB_H	619	#define ECB_H
515		620
516	/* 16 bits major, 16 bits minor */	621	/* 16 bits major, 16 bits minor */
517	#define ECB_VERSION 0x00010003	622	#define ECB_VERSION 0x00010006
518		623
519	#ifdef _WIN32	624	#ifdef _WIN32
520	typedef signed char int8_t;	625	typedef signed char int8_t;
521	typedef unsigned char uint8_t;	626	typedef unsigned char uint8_t;
522	typedef signed short int16_t;	627	typedef signed short int16_t;
…		…
539	typedef uint32_t uintptr_t;	644	typedef uint32_t uintptr_t;
540	typedef int32_t intptr_t;	645	typedef int32_t intptr_t;
541	#endif	646	#endif
542	#else	647	#else
543	#include <inttypes.h>	648	#include <inttypes.h>
544	#if UINTMAX_MAX > 0xffffffffU	649	#if (defined INTPTR_MAX ? INTPTR_MAX : ULONG_MAX) > 0xffffffffU
545	#define ECB_PTRSIZE 8	650	#define ECB_PTRSIZE 8
546	#else	651	#else
547	#define ECB_PTRSIZE 4	652	#define ECB_PTRSIZE 4
548	#endif	653	#endif
549	#endif	654	#endif
550		655
		656	#define ECB_GCC_AMD64 (__amd64 || __amd64__ || __x86_64 || __x86_64__)
		657	#define ECB_MSVC_AMD64 (_M_AMD64 || _M_X64)
		658
551	/* work around x32 idiocy by defining proper macros */	659	/* work around x32 idiocy by defining proper macros */
552	#if __x86_64 || _M_AMD64	660	#if ECB_GCC_AMD64 || ECB_MSVC_AMD64
553	#if _ILP32	661	#if _ILP32
554	#define ECB_AMD64_X32 1	662	#define ECB_AMD64_X32 1
555	#else	663	#else
556	#define ECB_AMD64 1	664	#define ECB_AMD64 1
557	#endif	665	#endif
…		…
562	* causing enormous grief in return for some better fake benchmark numbers.	670	* causing enormous grief in return for some better fake benchmark numbers.
563	* or so.	671	* or so.
564	* we try to detect these and simply assume they are not gcc - if they have	672	* we try to detect these and simply assume they are not gcc - if they have
565	* an issue with that they should have done it right in the first place.	673	* an issue with that they should have done it right in the first place.
566	*/	674	*/
567	#ifndef ECB_GCC_VERSION
568	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__	675	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__
569	#define ECB_GCC_VERSION(major,minor) 0	676	#define ECB_GCC_VERSION(major,minor) 0
570	#else	677	#else
571	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))	678	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))
572	#endif	679	#endif
573	#endif
574		680
575	#define ECB_C (__STDC__+0) /* this assumes that __STDC__ is either empty or a number */	681	#define ECB_CLANG_VERSION(major,minor) (__clang_major__ > (major) || (__clang_major__ == (major) && __clang_minor__ >= (minor)))
576	#define ECB_C99 (__STDC_VERSION__ >= 199901L)	682
577	#define ECB_C11 (__STDC_VERSION__ >= 201112L)	683	#if __clang__ && defined __has_builtin
		684	#define ECB_CLANG_BUILTIN(x) __has_builtin (x)
		685	#else
		686	#define ECB_CLANG_BUILTIN(x) 0
		687	#endif
		688
		689	#if __clang__ && defined __has_extension
		690	#define ECB_CLANG_EXTENSION(x) __has_extension (x)
		691	#else
		692	#define ECB_CLANG_EXTENSION(x) 0
		693	#endif
		694
578	#define ECB_CPP (__cplusplus+0)	695	#define ECB_CPP (__cplusplus+0)
579	#define ECB_CPP11 (__cplusplus >= 201103L)	696	#define ECB_CPP11 (__cplusplus >= 201103L)
		697	#define ECB_CPP14 (__cplusplus >= 201402L)
		698	#define ECB_CPP17 (__cplusplus >= 201703L)
		699
		700	#if ECB_CPP
		701	#define ECB_C 0
		702	#define ECB_STDC_VERSION 0
		703	#else
		704	#define ECB_C 1
		705	#define ECB_STDC_VERSION __STDC_VERSION__
		706	#endif
		707
		708	#define ECB_C99 (ECB_STDC_VERSION >= 199901L)
		709	#define ECB_C11 (ECB_STDC_VERSION >= 201112L)
		710	#define ECB_C17 (ECB_STDC_VERSION >= 201710L)
580		711
581	#if ECB_CPP	712	#if ECB_CPP
582	#define ECB_EXTERN_C extern "C"	713	#define ECB_EXTERN_C extern "C"
583	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {	714	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {
584	#define ECB_EXTERN_C_END }	715	#define ECB_EXTERN_C_END }
…		…
599		730
600	#if ECB_NO_SMP	731	#if ECB_NO_SMP
601	#define ECB_MEMORY_FENCE do { } while (0)	732	#define ECB_MEMORY_FENCE do { } while (0)
602	#endif	733	#endif
603		734
		735	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/compiler_ref/compiler_builtins.html */
		736	#if __xlC__ && ECB_CPP
		737	#include <builtins.h>
		738	#endif
		739
		740	#if 1400 <= _MSC_VER
		741	#include <intrin.h> /* fence functions _ReadBarrier, also bit search functions _BitScanReverse */
		742	#endif
		743
604	#ifndef ECB_MEMORY_FENCE	744	#ifndef ECB_MEMORY_FENCE
605	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	745	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
		746	#define ECB_MEMORY_FENCE_RELAXED __asm__ __volatile__ ("" : : : "memory")
606	#if __i386 || __i386__	747	#if __i386 || __i386__
607	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")	748	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")
608	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")	749	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
609	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	750	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
610	#elif __amd64 || __amd64__ || __x86_64 || __x86_64__	751	#elif ECB_GCC_AMD64
611	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")	752	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")
612	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")	753	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
613	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	754	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
614	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__	755	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__
615	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")	756	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")
		757	#elif defined __ARM_ARCH_2__ \
		758	|| defined __ARM_ARCH_3__ || defined __ARM_ARCH_3M__ \
		759	|| defined __ARM_ARCH_4__ || defined __ARM_ARCH_4T__ \
		760	|| defined __ARM_ARCH_5__ || defined __ARM_ARCH_5E__ \
		761	|| defined __ARM_ARCH_5T__ || defined __ARM_ARCH_5TE__ \
		762	|| defined __ARM_ARCH_5TEJ__
		763	/* should not need any, unless running old code on newer cpu - arm doesn't support that */
616	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \	764	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \
617	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__	765	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__ \
		766	|| defined __ARM_ARCH_6T2__
618	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")	767	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")
619	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \	768	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \
620	|| defined __ARM_ARCH_7M__ || defined __ARM_ARCH_7R__	769	|| defined __ARM_ARCH_7R__ || defined __ARM_ARCH_7M__
621	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")	770	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")
622	#elif __sparc || __sparc__	771	#elif __aarch64__
		772	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb ish" : : : "memory")
		773	#elif (__sparc || __sparc__) && !(__sparc_v8__ || defined __sparcv8)
623	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")	774	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")
624	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")	775	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")
625	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")	776	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")
626	#elif defined __s390__ || defined __s390x__	777	#elif defined __s390__ || defined __s390x__
627	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")	778	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")
…		…
648		799
649	#ifndef ECB_MEMORY_FENCE	800	#ifndef ECB_MEMORY_FENCE
650	#if ECB_GCC_VERSION(4,7)	801	#if ECB_GCC_VERSION(4,7)
651	/* see comment below (stdatomic.h) about the C11 memory model. */	802	/* see comment below (stdatomic.h) about the C11 memory model. */
652	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)	803	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)
		804	#define ECB_MEMORY_FENCE_ACQUIRE __atomic_thread_fence (__ATOMIC_ACQUIRE)
		805	#define ECB_MEMORY_FENCE_RELEASE __atomic_thread_fence (__ATOMIC_RELEASE)
		806	#define ECB_MEMORY_FENCE_RELAXED __atomic_thread_fence (__ATOMIC_RELAXED)
653		807
654	/* The __has_feature syntax from clang is so misdesigned that we cannot use it	808	#elif ECB_CLANG_EXTENSION(c_atomic)
655	* without risking compile time errors with other compilers. We *could*
656	* define our own ecb_clang_has_feature, but I just can't be bothered to work
657	* around this shit time and again.
658	* #elif defined __clang && __has_feature (cxx_atomic)
659	* // see comment below (stdatomic.h) about the C11 memory model.	809	/* see comment below (stdatomic.h) about the C11 memory model. */
660	* #define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)	810	#define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)
661	*/	811	#define ECB_MEMORY_FENCE_ACQUIRE __c11_atomic_thread_fence (__ATOMIC_ACQUIRE)
		812	#define ECB_MEMORY_FENCE_RELEASE __c11_atomic_thread_fence (__ATOMIC_RELEASE)
		813	#define ECB_MEMORY_FENCE_RELAXED __c11_atomic_thread_fence (__ATOMIC_RELAXED)
662		814
663	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__	815	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__
664	#define ECB_MEMORY_FENCE __sync_synchronize ()	816	#define ECB_MEMORY_FENCE __sync_synchronize ()
		817	#elif _MSC_VER >= 1500 /* VC++ 2008 */
		818	/* apparently, microsoft broke all the memory barrier stuff in Visual Studio 2008... */
		819	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)
		820	#define ECB_MEMORY_FENCE _ReadWriteBarrier (); MemoryBarrier()
		821	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier (); MemoryBarrier() /* according to msdn, _ReadBarrier is not a load fence */
		822	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier (); MemoryBarrier()
665	#elif _MSC_VER >= 1400 /* VC++ 2005 */	823	#elif _MSC_VER >= 1400 /* VC++ 2005 */
666	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)	824	#pragma intrinsic(_ReadBarrier,_WriteBarrier,_ReadWriteBarrier)
667	#define ECB_MEMORY_FENCE _ReadWriteBarrier ()	825	#define ECB_MEMORY_FENCE _ReadWriteBarrier ()
668	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier () /* according to msdn, _ReadBarrier is not a load fence */	826	#define ECB_MEMORY_FENCE_ACQUIRE _ReadWriteBarrier () /* according to msdn, _ReadBarrier is not a load fence */
669	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier ()	827	#define ECB_MEMORY_FENCE_RELEASE _WriteBarrier ()
670	#elif defined _WIN32	828	#elif defined _WIN32
671	#include <WinNT.h>	829	#include <WinNT.h>
672	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */	830	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */
673	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	831	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
674	#include <mbarrier.h>	832	#include <mbarrier.h>
675	#define ECB_MEMORY_FENCE __machine_rw_barrier ()	833	#define ECB_MEMORY_FENCE __machine_rw_barrier ()
676	#define ECB_MEMORY_FENCE_ACQUIRE __machine_r_barrier ()	834	#define ECB_MEMORY_FENCE_ACQUIRE __machine_acq_barrier ()
677	#define ECB_MEMORY_FENCE_RELEASE __machine_w_barrier ()	835	#define ECB_MEMORY_FENCE_RELEASE __machine_rel_barrier ()
		836	#define ECB_MEMORY_FENCE_RELAXED __compiler_barrier ()
678	#elif __xlC__	837	#elif __xlC__
679	#define ECB_MEMORY_FENCE __sync ()	838	#define ECB_MEMORY_FENCE __sync ()
680	#endif	839	#endif
681	#endif	840	#endif
682		841
683	#ifndef ECB_MEMORY_FENCE	842	#ifndef ECB_MEMORY_FENCE
684	#if ECB_C11 && !defined __STDC_NO_ATOMICS__	843	#if ECB_C11 && !defined __STDC_NO_ATOMICS__
685	/* we assume that these memory fences work on all variables/all memory accesses, */	844	/* we assume that these memory fences work on all variables/all memory accesses, */
686	/* not just C11 atomics and atomic accesses */	845	/* not just C11 atomics and atomic accesses */
687	#include <stdatomic.h>	846	#include <stdatomic.h>
688	/* Unfortunately, neither gcc 4.7 nor clang 3.1 generate any instructions for */
689	/* any fence other than seq_cst, which isn't very efficient for us. */
690	/* Why that is, we don't know - either the C11 memory model is quite useless */
691	/* for most usages, or gcc and clang have a bug */
692	/* I *currently* lean towards the latter, and inefficiently implement */
693	/* all three of ecb's fences as a seq_cst fence */
694	#define ECB_MEMORY_FENCE atomic_thread_fence (memory_order_seq_cst)	847	#define ECB_MEMORY_FENCE atomic_thread_fence (memory_order_seq_cst)
		848	#define ECB_MEMORY_FENCE_ACQUIRE atomic_thread_fence (memory_order_acquire)
		849	#define ECB_MEMORY_FENCE_RELEASE atomic_thread_fence (memory_order_release)
695	#endif	850	#endif
696	#endif	851	#endif
697		852
698	#ifndef ECB_MEMORY_FENCE	853	#ifndef ECB_MEMORY_FENCE
699	#if !ECB_AVOID_PTHREADS	854	#if !ECB_AVOID_PTHREADS
…		…
719		874
720	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE	875	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE
721	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	876	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
722	#endif	877	#endif
723		878
		879	#if !defined ECB_MEMORY_FENCE_RELAXED && defined ECB_MEMORY_FENCE
		880	#define ECB_MEMORY_FENCE_RELAXED ECB_MEMORY_FENCE /* very heavy-handed */
		881	#endif
		882
724	/*****************************************************************************/	883	/*****************************************************************************/
725		884
726	#if __cplusplus	885	#if ECB_CPP
727	#define ecb_inline static inline	886	#define ecb_inline static inline
728	#elif ECB_GCC_VERSION(2,5)	887	#elif ECB_GCC_VERSION(2,5)
729	#define ecb_inline static __inline__	888	#define ecb_inline static __inline__
730	#elif ECB_C99	889	#elif ECB_C99
731	#define ecb_inline static inline	890	#define ecb_inline static inline
…		…
745		904
746	#define ECB_CONCAT_(a, b) a ## b	905	#define ECB_CONCAT_(a, b) a ## b
747	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)	906	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)
748	#define ECB_STRINGIFY_(a) # a	907	#define ECB_STRINGIFY_(a) # a
749	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)	908	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)
		909	#define ECB_STRINGIFY_EXPR(expr) ((expr), ECB_STRINGIFY_ (expr))
750		910
751	#define ecb_function_ ecb_inline	911	#define ecb_function_ ecb_inline
752		912
753	#if ECB_GCC_VERSION(3,1)	913	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_VERSION(2,8)
754	#define ecb_attribute(attrlist) __attribute__(attrlist)	914	#define ecb_attribute(attrlist) __attribute__ (attrlist)
		915	#else
		916	#define ecb_attribute(attrlist)
		917	#endif
		918
		919	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_constant_p)
755	#define ecb_is_constant(expr) __builtin_constant_p (expr)	920	#define ecb_is_constant(expr) __builtin_constant_p (expr)
		921	#else
		922	/* possible C11 impl for integral types
		923	typedef struct ecb_is_constant_struct ecb_is_constant_struct;
		924	#define ecb_is_constant(expr) _Generic ((1 ? (struct ecb_is_constant_struct *)0 : (void *)((expr) - (expr)), ecb_is_constant_struct *: 0, default: 1)) */
		925
		926	#define ecb_is_constant(expr) 0
		927	#endif
		928
		929	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_expect)
756	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))	930	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))
		931	#else
		932	#define ecb_expect(expr,value) (expr)
		933	#endif
		934
		935	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_prefetch)
757	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)	936	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)
758	#else	937	#else
759	#define ecb_attribute(attrlist)
760	#define ecb_is_constant(expr) 0
761	#define ecb_expect(expr,value) (expr)
762	#define ecb_prefetch(addr,rw,locality)	938	#define ecb_prefetch(addr,rw,locality)
763	#endif	939	#endif
764		940
765	/* no emulation for ecb_decltype */	941	/* no emulation for ecb_decltype */
766	#if ECB_GCC_VERSION(4,5)	942	#if ECB_CPP11
		943	// older implementations might have problems with decltype(x)::type, work around it
		944	template<class T> struct ecb_decltype_t { typedef T type; };
767	#define ecb_decltype(x) __decltype(x)	945	#define ecb_decltype(x) ecb_decltype_t<decltype (x)>::type
768	#elif ECB_GCC_VERSION(3,0)	946	#elif ECB_GCC_VERSION(3,0) || ECB_CLANG_VERSION(2,8)
769	#define ecb_decltype(x) __typeof(x)	947	#define ecb_decltype(x) __typeof__ (x)
770	#endif	948	#endif
771		949
		950	#if _MSC_VER >= 1300
		951	#define ecb_deprecated __declspec (deprecated)
		952	#else
		953	#define ecb_deprecated ecb_attribute ((__deprecated__))
		954	#endif
		955
		956	#if _MSC_VER >= 1500
		957	#define ecb_deprecated_message(msg) __declspec (deprecated (msg))
		958	#elif ECB_GCC_VERSION(4,5)
		959	#define ecb_deprecated_message(msg) ecb_attribute ((__deprecated__ (msg))
		960	#else
		961	#define ecb_deprecated_message(msg) ecb_deprecated
		962	#endif
		963
		964	#if _MSC_VER >= 1400
		965	#define ecb_noinline __declspec (noinline)
		966	#else
772	#define ecb_noinline ecb_attribute ((__noinline__))	967	#define ecb_noinline ecb_attribute ((__noinline__))
		968	#endif
		969
773	#define ecb_unused ecb_attribute ((__unused__))	970	#define ecb_unused ecb_attribute ((__unused__))
774	#define ecb_const ecb_attribute ((__const__))	971	#define ecb_const ecb_attribute ((__const__))
775	#define ecb_pure ecb_attribute ((__pure__))	972	#define ecb_pure ecb_attribute ((__pure__))
776		973
777	#if ECB_C11	974	#if ECB_C11 || __IBMC_NORETURN
		975	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/language_ref/noreturn.html */
778	#define ecb_noreturn _Noreturn	976	#define ecb_noreturn _Noreturn
		977	#elif ECB_CPP11
		978	#define ecb_noreturn [[noreturn]]
		979	#elif _MSC_VER >= 1200
		980	/* http://msdn.microsoft.com/en-us/library/k6ktzx3s.aspx */
		981	#define ecb_noreturn __declspec (noreturn)
779	#else	982	#else
780	#define ecb_noreturn ecb_attribute ((__noreturn__))	983	#define ecb_noreturn ecb_attribute ((__noreturn__))
781	#endif	984	#endif
782		985
783	#if ECB_GCC_VERSION(4,3)	986	#if ECB_GCC_VERSION(4,3)
…		…
798	/* for compatibility to the rest of the world */	1001	/* for compatibility to the rest of the world */
799	#define ecb_likely(expr) ecb_expect_true (expr)	1002	#define ecb_likely(expr) ecb_expect_true (expr)
800	#define ecb_unlikely(expr) ecb_expect_false (expr)	1003	#define ecb_unlikely(expr) ecb_expect_false (expr)
801		1004
802	/* count trailing zero bits and count # of one bits */	1005	/* count trailing zero bits and count # of one bits */
803	#if ECB_GCC_VERSION(3,4)	1006	#if ECB_GCC_VERSION(3,4) \
		1007	|| (ECB_CLANG_BUILTIN(__builtin_clz) && ECB_CLANG_BUILTIN(__builtin_clzll) \
		1008	&& ECB_CLANG_BUILTIN(__builtin_ctz) && ECB_CLANG_BUILTIN(__builtin_ctzll) \
		1009	&& ECB_CLANG_BUILTIN(__builtin_popcount))
804	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */	1010	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */
805	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)	1011	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)
806	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)	1012	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)
807	#define ecb_ctz32(x) __builtin_ctz (x)	1013	#define ecb_ctz32(x) __builtin_ctz (x)
808	#define ecb_ctz64(x) __builtin_ctzll (x)	1014	#define ecb_ctz64(x) __builtin_ctzll (x)
809	#define ecb_popcount32(x) __builtin_popcount (x)	1015	#define ecb_popcount32(x) __builtin_popcount (x)
810	/* no popcountll */	1016	/* no popcountll */
811	#else	1017	#else
812	ecb_function_ int ecb_ctz32 (uint32_t x) ecb_const;	1018	ecb_function_ ecb_const int ecb_ctz32 (uint32_t x);
813	ecb_function_ int	1019	ecb_function_ ecb_const int
814	ecb_ctz32 (uint32_t x)	1020	ecb_ctz32 (uint32_t x)
815	{	1021	{
		1022	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		1023	unsigned long r;
		1024	_BitScanForward (&r, x);
		1025	return (int)r;
		1026	#else
816	int r = 0;	1027	int r = 0;
817		1028
818	x &= ~x + 1; /* this isolates the lowest bit */	1029	x &= ~x + 1; /* this isolates the lowest bit */
819		1030
820	#if ECB_branchless_on_i386	1031	#if ECB_branchless_on_i386
…		…
830	if (x & 0xff00ff00) r += 8;	1041	if (x & 0xff00ff00) r += 8;
831	if (x & 0xffff0000) r += 16;	1042	if (x & 0xffff0000) r += 16;
832	#endif	1043	#endif
833		1044
834	return r;	1045	return r;
		1046	#endif
835	}	1047	}
836		1048
837	ecb_function_ int ecb_ctz64 (uint64_t x) ecb_const;	1049	ecb_function_ ecb_const int ecb_ctz64 (uint64_t x);
838	ecb_function_ int	1050	ecb_function_ ecb_const int
839	ecb_ctz64 (uint64_t x)	1051	ecb_ctz64 (uint64_t x)
840	{	1052	{
		1053	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1054	unsigned long r;
		1055	_BitScanForward64 (&r, x);
		1056	return (int)r;
		1057	#else
841	int shift = x & 0xffffffffU ? 0 : 32;	1058	int shift = x & 0xffffffff ? 0 : 32;
842	return ecb_ctz32 (x >> shift) + shift;	1059	return ecb_ctz32 (x >> shift) + shift;
		1060	#endif
843	}	1061	}
844		1062
845	ecb_function_ int ecb_popcount32 (uint32_t x) ecb_const;	1063	ecb_function_ ecb_const int ecb_popcount32 (uint32_t x);
846	ecb_function_ int	1064	ecb_function_ ecb_const int
847	ecb_popcount32 (uint32_t x)	1065	ecb_popcount32 (uint32_t x)
848	{	1066	{
849	x -= (x >> 1) & 0x55555555;	1067	x -= (x >> 1) & 0x55555555;
850	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);	1068	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);
851	x = ((x >> 4) + x) & 0x0f0f0f0f;	1069	x = ((x >> 4) + x) & 0x0f0f0f0f;
852	x *= 0x01010101;	1070	x *= 0x01010101;
853		1071
854	return x >> 24;	1072	return x >> 24;
855	}	1073	}
856		1074
857	ecb_function_ int ecb_ld32 (uint32_t x) ecb_const;	1075	ecb_function_ ecb_const int ecb_ld32 (uint32_t x);
858	ecb_function_ int ecb_ld32 (uint32_t x)	1076	ecb_function_ ecb_const int ecb_ld32 (uint32_t x)
859	{	1077	{
		1078	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		1079	unsigned long r;
		1080	_BitScanReverse (&r, x);
		1081	return (int)r;
		1082	#else
860	int r = 0;	1083	int r = 0;
861		1084
862	if (x >> 16) { x >>= 16; r += 16; }	1085	if (x >> 16) { x >>= 16; r += 16; }
863	if (x >> 8) { x >>= 8; r += 8; }	1086	if (x >> 8) { x >>= 8; r += 8; }
864	if (x >> 4) { x >>= 4; r += 4; }	1087	if (x >> 4) { x >>= 4; r += 4; }
865	if (x >> 2) { x >>= 2; r += 2; }	1088	if (x >> 2) { x >>= 2; r += 2; }
866	if (x >> 1) { r += 1; }	1089	if (x >> 1) { r += 1; }
867		1090
868	return r;	1091	return r;
		1092	#endif
869	}	1093	}
870		1094
871	ecb_function_ int ecb_ld64 (uint64_t x) ecb_const;	1095	ecb_function_ ecb_const int ecb_ld64 (uint64_t x);
872	ecb_function_ int ecb_ld64 (uint64_t x)	1096	ecb_function_ ecb_const int ecb_ld64 (uint64_t x)
873	{	1097	{
		1098	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1099	unsigned long r;
		1100	_BitScanReverse64 (&r, x);
		1101	return (int)r;
		1102	#else
874	int r = 0;	1103	int r = 0;
875		1104
876	if (x >> 32) { x >>= 32; r += 32; }	1105	if (x >> 32) { x >>= 32; r += 32; }
877		1106
878	return r + ecb_ld32 (x);	1107	return r + ecb_ld32 (x);
		1108	#endif
879	}	1109	}
880	#endif	1110	#endif
881		1111
882	ecb_function_ ecb_bool ecb_is_pot32 (uint32_t x) ecb_const;	1112	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x);
883	ecb_function_ ecb_bool ecb_is_pot32 (uint32_t x) { return !(x & (x - 1)); }	1113	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x) { return !(x & (x - 1)); }
884	ecb_function_ ecb_bool ecb_is_pot64 (uint64_t x) ecb_const;	1114	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x);
885	ecb_function_ ecb_bool ecb_is_pot64 (uint64_t x) { return !(x & (x - 1)); }	1115	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x) { return !(x & (x - 1)); }
886		1116
887	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x) ecb_const;	1117	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x);
888	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x)	1118	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x)
889	{	1119	{
890	return ( (x * 0x0802U & 0x22110U)	1120	return ( (x * 0x0802U & 0x22110U)
891	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;	1121	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;
892	}	1122	}
893		1123
894	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x) ecb_const;	1124	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x);
895	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x)	1125	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x)
896	{	1126	{
897	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);	1127	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);
898	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);	1128	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);
899	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);	1129	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);
900	x = ( x >> 8 ) | ( x << 8);	1130	x = ( x >> 8 ) | ( x << 8);
901		1131
902	return x;	1132	return x;
903	}	1133	}
904		1134
905	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x) ecb_const;	1135	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x);
906	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x)	1136	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x)
907	{	1137	{
908	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);	1138	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);
909	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);	1139	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);
910	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);	1140	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);
911	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);	1141	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);
…		…
914	return x;	1144	return x;
915	}	1145	}
916		1146
917	/* popcount64 is only available on 64 bit cpus as gcc builtin */	1147	/* popcount64 is only available on 64 bit cpus as gcc builtin */
918	/* so for this version we are lazy */	1148	/* so for this version we are lazy */
919	ecb_function_ int ecb_popcount64 (uint64_t x) ecb_const;	1149	ecb_function_ ecb_const int ecb_popcount64 (uint64_t x);
920	ecb_function_ int	1150	ecb_function_ ecb_const int
921	ecb_popcount64 (uint64_t x)	1151	ecb_popcount64 (uint64_t x)
922	{	1152	{
923	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);	1153	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);
924	}	1154	}
925		1155
926	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) ecb_const;	1156	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count);
927	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) ecb_const;	1157	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count);
928	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) ecb_const;	1158	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count);
929	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) ecb_const;	1159	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count);
930	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) ecb_const;	1160	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count);
931	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) ecb_const;	1161	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count);
932	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) ecb_const;	1162	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count);
933	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) ecb_const;	1163	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count);
934		1164
935	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }	1165	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }
936	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }	1166	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }
937	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }	1167	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }
938	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }	1168	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }
939	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }	1169	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }
940	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }	1170	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }
941	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }	1171	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }
942	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }	1172	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }
943		1173
944	#if ECB_GCC_VERSION(4,3)	1174	#if ECB_GCC_VERSION(4,3) || (ECB_CLANG_BUILTIN(__builtin_bswap32) && ECB_CLANG_BUILTIN(__builtin_bswap64))
		1175	#if ECB_GCC_VERSION(4,8) || ECB_CLANG_BUILTIN(__builtin_bswap16)
		1176	#define ecb_bswap16(x) __builtin_bswap16 (x)
		1177	#else
945	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)	1178	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)
		1179	#endif
946	#define ecb_bswap32(x) __builtin_bswap32 (x)	1180	#define ecb_bswap32(x) __builtin_bswap32 (x)
947	#define ecb_bswap64(x) __builtin_bswap64 (x)	1181	#define ecb_bswap64(x) __builtin_bswap64 (x)
		1182	#elif _MSC_VER
		1183	#include <stdlib.h>
		1184	#define ecb_bswap16(x) ((uint16_t)_byteswap_ushort ((uint16_t)(x)))
		1185	#define ecb_bswap32(x) ((uint32_t)_byteswap_ulong ((uint32_t)(x)))
		1186	#define ecb_bswap64(x) ((uint64_t)_byteswap_uint64 ((uint64_t)(x)))
948	#else	1187	#else
949	ecb_function_ uint16_t ecb_bswap16 (uint16_t x) ecb_const;	1188	ecb_function_ ecb_const uint16_t ecb_bswap16 (uint16_t x);
950	ecb_function_ uint16_t	1189	ecb_function_ ecb_const uint16_t
951	ecb_bswap16 (uint16_t x)	1190	ecb_bswap16 (uint16_t x)
952	{	1191	{
953	return ecb_rotl16 (x, 8);	1192	return ecb_rotl16 (x, 8);
954	}	1193	}
955		1194
956	ecb_function_ uint32_t ecb_bswap32 (uint32_t x) ecb_const;	1195	ecb_function_ ecb_const uint32_t ecb_bswap32 (uint32_t x);
957	ecb_function_ uint32_t	1196	ecb_function_ ecb_const uint32_t
958	ecb_bswap32 (uint32_t x)	1197	ecb_bswap32 (uint32_t x)
959	{	1198	{
960	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);	1199	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);
961	}	1200	}
962		1201
963	ecb_function_ uint64_t ecb_bswap64 (uint64_t x) ecb_const;	1202	ecb_function_ ecb_const uint64_t ecb_bswap64 (uint64_t x);
964	ecb_function_ uint64_t	1203	ecb_function_ ecb_const uint64_t
965	ecb_bswap64 (uint64_t x)	1204	ecb_bswap64 (uint64_t x)
966	{	1205	{
967	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);	1206	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);
968	}	1207	}
969	#endif	1208	#endif
970		1209
971	#if ECB_GCC_VERSION(4,5)	1210	#if ECB_GCC_VERSION(4,5) || ECB_CLANG_BUILTIN(__builtin_unreachable)
972	#define ecb_unreachable() __builtin_unreachable ()	1211	#define ecb_unreachable() __builtin_unreachable ()
973	#else	1212	#else
974	/* this seems to work fine, but gcc always emits a warning for it :/ */	1213	/* this seems to work fine, but gcc always emits a warning for it :/ */
975	ecb_inline void ecb_unreachable (void) ecb_noreturn;	1214	ecb_inline ecb_noreturn void ecb_unreachable (void);
976	ecb_inline void ecb_unreachable (void) { }	1215	ecb_inline ecb_noreturn void ecb_unreachable (void) { }
977	#endif	1216	#endif
978		1217
979	/* try to tell the compiler that some condition is definitely true */	1218	/* try to tell the compiler that some condition is definitely true */
980	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0	1219	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0
981		1220
982	ecb_inline unsigned char ecb_byteorder_helper (void) ecb_const;	1221	ecb_inline ecb_const uint32_t ecb_byteorder_helper (void);
983	ecb_inline unsigned char	1222	ecb_inline ecb_const uint32_t
984	ecb_byteorder_helper (void)	1223	ecb_byteorder_helper (void)
985	{	1224	{
986	/* the union code still generates code under pressure in gcc, */	1225	/* the union code still generates code under pressure in gcc, */
987	/* but less than using pointers, and always seems to */	1226	/* but less than using pointers, and always seems to */
988	/* successfully return a constant. */	1227	/* successfully return a constant. */
989	/* the reason why we have this horrible preprocessor mess */	1228	/* the reason why we have this horrible preprocessor mess */
990	/* is to avoid it in all cases, at least on common architectures */	1229	/* is to avoid it in all cases, at least on common architectures */
991	/* or when using a recent enough gcc version (>= 4.6) */	1230	/* or when using a recent enough gcc version (>= 4.6) */
992	#if __i386 || __i386__ || _M_X86 || __amd64 || __amd64__ || _M_X64
993	return 0x44;
994	#elif __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_LITTLE_ENDIAN__	1231	#if (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_LITTLE_ENDIAN__) \
		1232	|| ((__i386 || __i386__ || _M_IX86 || ECB_GCC_AMD64 || ECB_MSVC_AMD64) && !__VOS__)
		1233	#define ECB_LITTLE_ENDIAN 1
995	return 0x44;	1234	return 0x44332211;
996	#elif __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__	1235	#elif (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__) \
		1236	|| ((__AARCH64EB__ || __MIPSEB__ || __ARMEB__) && !__VOS__)
		1237	#define ECB_BIG_ENDIAN 1
997	return 0x11;	1238	return 0x11223344;
998	#else	1239	#else
999	union	1240	union
1000	{	1241	{
		1242	uint8_t c[4];
1001	uint32_t i;	1243	uint32_t u;
1002	uint8_t c;
1003	} u = { 0x11223344 };	1244	} u = { 0x11, 0x22, 0x33, 0x44 };
1004	return u.c;	1245	return u.u;
1005	#endif	1246	#endif
1006	}	1247	}
1007		1248
1008	ecb_inline ecb_bool ecb_big_endian (void) ecb_const;	1249	ecb_inline ecb_const ecb_bool ecb_big_endian (void);
1009	ecb_inline ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11; }	1250	ecb_inline ecb_const ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11223344; }
1010	ecb_inline ecb_bool ecb_little_endian (void) ecb_const;	1251	ecb_inline ecb_const ecb_bool ecb_little_endian (void);
1011	ecb_inline ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44; }	1252	ecb_inline ecb_const ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44332211; }
1012		1253
1013	#if ECB_GCC_VERSION(3,0) || ECB_C99	1254	#if ECB_GCC_VERSION(3,0) || ECB_C99
1014	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))	1255	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))
1015	#else	1256	#else
1016	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))	1257	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))
1017	#endif	1258	#endif
1018		1259
1019	#if __cplusplus	1260	#if ECB_CPP
1020	template<typename T>	1261	template<typename T>
1021	static inline T ecb_div_rd (T val, T div)	1262	static inline T ecb_div_rd (T val, T div)
1022	{	1263	{
1023	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;	1264	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;
1024	}	1265	}
…		…
1041	}	1282	}
1042	#else	1283	#else
1043	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))	1284	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))
1044	#endif	1285	#endif
1045		1286
		1287	ecb_function_ ecb_const uint32_t ecb_binary16_to_binary32 (uint32_t x);
		1288	ecb_function_ ecb_const uint32_t
		1289	ecb_binary16_to_binary32 (uint32_t x)
		1290	{
		1291	unsigned int s = (x & 0x8000) << (31 - 15);
		1292	int e = (x >> 10) & 0x001f;
		1293	unsigned int m = x & 0x03ff;
		1294
		1295	if (ecb_expect_false (e == 31))
		1296	/* infinity or NaN */
		1297	e = 255 - (127 - 15);
		1298	else if (ecb_expect_false (!e))
		1299	{
		1300	if (ecb_expect_true (!m))
		1301	/* zero, handled by code below by forcing e to 0 */
		1302	e = 0 - (127 - 15);
		1303	else
		1304	{
		1305	/* subnormal, renormalise */
		1306	unsigned int s = 10 - ecb_ld32 (m);
		1307
		1308	m = (m << s) & 0x3ff; /* mask implicit bit */
		1309	e -= s - 1;
		1310	}
		1311	}
		1312
		1313	/* e and m now are normalised, or zero, (or inf or nan) */
		1314	e += 127 - 15;
		1315
		1316	return s | (e << 23) | (m << (23 - 10));
		1317	}
		1318
		1319	ecb_function_ ecb_const uint16_t ecb_binary32_to_binary16 (uint32_t x);
		1320	ecb_function_ ecb_const uint16_t
		1321	ecb_binary32_to_binary16 (uint32_t x)
		1322	{
		1323	unsigned int s = (x >> 16) & 0x00008000; /* sign bit, the easy part */
		1324	unsigned int e = ((x >> 23) & 0x000000ff) - (127 - 15); /* the desired exponent */
		1325	unsigned int m = x & 0x007fffff;
		1326
		1327	x &= 0x7fffffff;
		1328
		1329	/* if it's within range of binary16 normals, use fast path */
		1330	if (ecb_expect_true (0x38800000 <= x && x <= 0x477fefff))
		1331	{
		1332	/* mantissa round-to-even */
		1333	m += 0x00000fff + ((m >> (23 - 10)) & 1);
		1334
		1335	/* handle overflow */
		1336	if (ecb_expect_false (m >= 0x00800000))
		1337	{
		1338	m >>= 1;
		1339	e += 1;
		1340	}
		1341
		1342	return s | (e << 10) | (m >> (23 - 10));
		1343	}
		1344
		1345	/* handle large numbers and infinity */
		1346	if (ecb_expect_true (0x477fefff < x && x <= 0x7f800000))
		1347	return s | 0x7c00;
		1348
		1349	/* handle zero, subnormals and small numbers */
		1350	if (ecb_expect_true (x < 0x38800000))
		1351	{
		1352	/* zero */
		1353	if (ecb_expect_true (!x))
		1354	return s;
		1355
		1356	/* handle subnormals */
		1357
		1358	/* too small, will be zero */
		1359	if (e < (14 - 24)) /* might not be sharp, but is good enough */
		1360	return s;
		1361
		1362	m |= 0x00800000; /* make implicit bit explicit */
		1363
		1364	/* very tricky - we need to round to the nearest e (+10) bit value */
		1365	{
		1366	unsigned int bits = 14 - e;
		1367	unsigned int half = (1 << (bits - 1)) - 1;
		1368	unsigned int even = (m >> bits) & 1;
		1369
		1370	/* if this overflows, we will end up with a normalised number */
		1371	m = (m + half + even) >> bits;
		1372	}
		1373
		1374	return s | m;
		1375	}
		1376
		1377	/* handle NaNs, preserve leftmost nan bits, but make sure we don't turn them into infinities */
		1378	m >>= 13;
		1379
		1380	return s | 0x7c00 | m | !m;
		1381	}
		1382
1046	/*******************************************************************************/	1383	/*******************************************************************************/
1047	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */	1384	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */
1048		1385
1049	/* basically, everything uses "ieee pure-endian" floating point numbers */	1386	/* basically, everything uses "ieee pure-endian" floating point numbers */
1050	/* the only noteworthy exception is ancient armle, which uses order 43218765 */	1387	/* the only noteworthy exception is ancient armle, which uses order 43218765 */
1051	#if 0 \	1388	#if 0 \
1052	|| __i386 || __i386__ \	1389	|| __i386 || __i386__ \
1053	|| __amd64 || __amd64__ || __x86_64 || __x86_64__ \	1390	|| ECB_GCC_AMD64 \
1054	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \	1391	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \
1055	|| defined __arm__ && defined __ARM_EABI__ \
1056	|| defined __s390__ || defined __s390x__ \	1392	|| defined __s390__ || defined __s390x__ \
1057	|| defined __mips__ \	1393	|| defined __mips__ \
1058	|| defined __alpha__ \	1394	|| defined __alpha__ \
1059	|| defined __hppa__ \	1395	|| defined __hppa__ \
1060	|| defined __ia64__ \	1396	|| defined __ia64__ \
1061	|| defined __m68k__ \	1397	|| defined __m68k__ \
1062	|| defined __m88k__ \	1398	|| defined __m88k__ \
1063	|| defined __sh__ \	1399	|| defined __sh__ \
1064	|| defined _M_IX86 || defined _M_AMD64 || defined _M_IA64	1400	|| defined _M_IX86 || defined ECB_MSVC_AMD64 || defined _M_IA64 \
		1401	|| (defined __arm__ && (defined __ARM_EABI__ || defined __EABI__ || defined __VFP_FP__ || defined _WIN32_WCE || defined __ANDROID__)) \
		1402	|| defined __aarch64__
1065	#define ECB_STDFP 1	1403	#define ECB_STDFP 1
1066	#include <string.h> /* for memcpy */	1404	#include <string.h> /* for memcpy */
1067	#else	1405	#else
1068	#define ECB_STDFP 0	1406	#define ECB_STDFP 0
1069	#endif	1407	#endif
1070		1408
1071	#ifndef ECB_NO_LIBM	1409	#ifndef ECB_NO_LIBM
1072		1410
1073	#include <math.h> /* for frexp*, ldexp*, INFINITY, NAN */	1411	#include <math.h> /* for frexp*, ldexp*, INFINITY, NAN */
1074		1412
		1413	/* only the oldest of old doesn't have this one. solaris. */
		1414	#ifdef INFINITY
		1415	#define ECB_INFINITY INFINITY
		1416	#else
		1417	#define ECB_INFINITY HUGE_VAL
		1418	#endif
		1419
1075	#ifdef NEN	1420	#ifdef NAN
1076	#define ECB_NAN NAN	1421	#define ECB_NAN NAN
1077	#else	1422	#else
1078	#define ECB_NAN INFINITY	1423	#define ECB_NAN ECB_INFINITY
1079	#endif	1424	#endif
1080		1425
1081	/* converts an ieee half/binary16 to a float */	1426	#if ECB_C99 || _XOPEN_VERSION >= 600 || _POSIX_VERSION >= 200112L
1082	ecb_function_ float ecb_binary16_to_float (uint16_t x) ecb_const;	1427	#define ecb_ldexpf(x,e) ldexpf ((x), (e))
1083	ecb_function_ float	1428	#define ecb_frexpf(x,e) frexpf ((x), (e))
1084	ecb_binary16_to_float (uint16_t x)	1429	#else
1085	{	1430	#define ecb_ldexpf(x,e) (float) ldexp ((double) (x), (e))
1086	int e = (x >> 10) & 0x1f;	1431	#define ecb_frexpf(x,e) (float) frexp ((double) (x), (e))
1087	int m = x & 0x3ff;	1432	#endif
1088	float r;
1089
1090	if (!e ) r = ldexpf (m , -24);
1091	else if (e != 31) r = ldexpf (m + 0x400, e - 25);
1092	else if (m ) r = ECB_NAN;
1093	else r = INFINITY;
1094
1095	return x & 0x8000 ? -r : r;
1096	}
1097		1433
1098	/* convert a float to ieee single/binary32 */	1434	/* convert a float to ieee single/binary32 */
1099	ecb_function_ uint32_t ecb_float_to_binary32 (float x) ecb_const;	1435	ecb_function_ ecb_const uint32_t ecb_float_to_binary32 (float x);
1100	ecb_function_ uint32_t	1436	ecb_function_ ecb_const uint32_t
1101	ecb_float_to_binary32 (float x)	1437	ecb_float_to_binary32 (float x)
1102	{	1438	{
1103	uint32_t r;	1439	uint32_t r;
1104		1440
1105	#if ECB_STDFP	1441	#if ECB_STDFP
…		…
1112	if (x == 0e0f ) return 0x00000000U;	1448	if (x == 0e0f ) return 0x00000000U;
1113	if (x > +3.40282346638528860e+38f) return 0x7f800000U;	1449	if (x > +3.40282346638528860e+38f) return 0x7f800000U;
1114	if (x < -3.40282346638528860e+38f) return 0xff800000U;	1450	if (x < -3.40282346638528860e+38f) return 0xff800000U;
1115	if (x != x ) return 0x7fbfffffU;	1451	if (x != x ) return 0x7fbfffffU;
1116		1452
1117	m = frexpf (x, &e) * 0x1000000U;	1453	m = ecb_frexpf (x, &e) * 0x1000000U;
1118		1454
1119	r = m & 0x80000000U;	1455	r = m & 0x80000000U;
1120		1456
1121	if (r)	1457	if (r)
1122	m = -m;	1458	m = -m;
…		…
1134		1470
1135	return r;	1471	return r;
1136	}	1472	}
1137		1473
1138	/* converts an ieee single/binary32 to a float */	1474	/* converts an ieee single/binary32 to a float */
1139	ecb_function_ float ecb_binary32_to_float (uint32_t x) ecb_const;	1475	ecb_function_ ecb_const float ecb_binary32_to_float (uint32_t x);
1140	ecb_function_ float	1476	ecb_function_ ecb_const float
1141	ecb_binary32_to_float (uint32_t x)	1477	ecb_binary32_to_float (uint32_t x)
1142	{	1478	{
1143	float r;	1479	float r;
1144		1480
1145	#if ECB_STDFP	1481	#if ECB_STDFP
…		…
1155	x |= 0x800000U;	1491	x |= 0x800000U;
1156	else	1492	else
1157	e = 1;	1493	e = 1;
1158		1494
1159	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */	1495	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */
1160	r = ldexpf (x * (0.5f / 0x800000U), e - 126);	1496	r = ecb_ldexpf (x * (0.5f / 0x800000U), e - 126);
1161		1497
1162	r = neg ? -r : r;	1498	r = neg ? -r : r;
1163	#endif	1499	#endif
1164		1500
1165	return r;	1501	return r;
1166	}	1502	}
1167		1503
1168	/* convert a double to ieee double/binary64 */	1504	/* convert a double to ieee double/binary64 */
1169	ecb_function_ uint64_t ecb_double_to_binary64 (double x) ecb_const;	1505	ecb_function_ ecb_const uint64_t ecb_double_to_binary64 (double x);
1170	ecb_function_ uint64_t	1506	ecb_function_ ecb_const uint64_t
1171	ecb_double_to_binary64 (double x)	1507	ecb_double_to_binary64 (double x)
1172	{	1508	{
1173	uint64_t r;	1509	uint64_t r;
1174		1510
1175	#if ECB_STDFP	1511	#if ECB_STDFP
…		…
1204		1540
1205	return r;	1541	return r;
1206	}	1542	}
1207		1543
1208	/* converts an ieee double/binary64 to a double */	1544	/* converts an ieee double/binary64 to a double */
1209	ecb_function_ double ecb_binary64_to_double (uint64_t x) ecb_const;	1545	ecb_function_ ecb_const double ecb_binary64_to_double (uint64_t x);
1210	ecb_function_ double	1546	ecb_function_ ecb_const double
1211	ecb_binary64_to_double (uint64_t x)	1547	ecb_binary64_to_double (uint64_t x)
1212	{	1548	{
1213	double r;	1549	double r;
1214		1550
1215	#if ECB_STDFP	1551	#if ECB_STDFP
…		…
1233	#endif	1569	#endif
1234		1570
1235	return r;	1571	return r;
1236	}	1572	}
1237		1573
		1574	/* convert a float to ieee half/binary16 */
		1575	ecb_function_ ecb_const uint16_t ecb_float_to_binary16 (float x);
		1576	ecb_function_ ecb_const uint16_t
		1577	ecb_float_to_binary16 (float x)
		1578	{
		1579	return ecb_binary32_to_binary16 (ecb_float_to_binary32 (x));
		1580	}
		1581
		1582	/* convert an ieee half/binary16 to float */
		1583	ecb_function_ ecb_const float ecb_binary16_to_float (uint16_t x);
		1584	ecb_function_ ecb_const float
		1585	ecb_binary16_to_float (uint16_t x)
		1586	{
		1587	return ecb_binary32_to_float (ecb_binary16_to_binary32 (x));
		1588	}
		1589
1238	#endif	1590	#endif
1239		1591
1240	#endif	1592	#endif
1241		1593
1242	/* ECB.H END */	1594	/* ECB.H END */
1243		1595
1244	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS	1596	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS
1245	/* if your architecture doesn't need memory fences, e.g. because it is	1597	/* if your architecture doesn't need memory fences, e.g. because it is
1246	* single-cpu/core, or if you use libev in a project that doesn't use libev	1598	* single-cpu/core, or if you use libev in a project that doesn't use libev
1247	* from multiple threads, then you can define ECB_AVOID_PTHREADS when compiling	1599	* from multiple threads, then you can define ECB_NO_THREADS when compiling
1248	* libev, in which cases the memory fences become nops.	1600	* libev, in which cases the memory fences become nops.
1249	* alternatively, you can remove this #error and link against libpthread,	1601	* alternatively, you can remove this #error and link against libpthread,
1250	* which will then provide the memory fences.	1602	* which will then provide the memory fences.
1251	*/	1603	*/
1252	# error "memory fences not defined for your architecture, please report"	1604	# error "memory fences not defined for your architecture, please report"
…		…
1256	# define ECB_MEMORY_FENCE do { } while (0)	1608	# define ECB_MEMORY_FENCE do { } while (0)
1257	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE	1609	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE
1258	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	1610	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
1259	#endif	1611	#endif
1260		1612
1261	#define expect_false(cond) ecb_expect_false (cond)
1262	#define expect_true(cond) ecb_expect_true (cond)
1263	#define noinline ecb_noinline
1264
1265	#define inline_size ecb_inline	1613	#define inline_size ecb_inline
1266		1614
1267	#if EV_FEATURE_CODE	1615	#if EV_FEATURE_CODE
1268	# define inline_speed ecb_inline	1616	# define inline_speed ecb_inline
1269	#else	1617	#else
1270	# define inline_speed static noinline	1618	# define inline_speed ecb_noinline static
1271	#endif	1619	#endif
		1620
		1621	/*****************************************************************************/
		1622	/* raw syscall wrappers */
		1623
		1624	#if EV_NEED_SYSCALL
		1625
		1626	#include <sys/syscall.h>
		1627
		1628	/*
		1629	* define some syscall wrappers for common architectures
		1630	* this is mostly for nice looks during debugging, not performance.
		1631	* our syscalls return < 0, not == -1, on error. which is good
		1632	* enough for linux aio.
		1633	* TODO: arm is also common nowadays, maybe even mips and x86
		1634	* TODO: after implementing this, it suddenly looks like overkill, but its hard to remove...
		1635	*/
		1636	#if __GNUC__ && __linux && ECB_AMD64 && !defined __OPTIMIZE_SIZE__
		1637	/* the costly errno access probably kills this for size optimisation */
		1638
		1639	#define ev_syscall(nr,narg,arg1,arg2,arg3,arg4,arg5,arg6) \
		1640	({ \
		1641	long res; \
		1642	register unsigned long r6 __asm__ ("r9" ); \
		1643	register unsigned long r5 __asm__ ("r8" ); \
		1644	register unsigned long r4 __asm__ ("r10"); \
		1645	register unsigned long r3 __asm__ ("rdx"); \
		1646	register unsigned long r2 __asm__ ("rsi"); \
		1647	register unsigned long r1 __asm__ ("rdi"); \
		1648	if (narg >= 6) r6 = (unsigned long)(arg6); \
		1649	if (narg >= 5) r5 = (unsigned long)(arg5); \
		1650	if (narg >= 4) r4 = (unsigned long)(arg4); \
		1651	if (narg >= 3) r3 = (unsigned long)(arg3); \
		1652	if (narg >= 2) r2 = (unsigned long)(arg2); \
		1653	if (narg >= 1) r1 = (unsigned long)(arg1); \
		1654	__asm__ __volatile__ ( \
		1655	"syscall\n\t" \
		1656	: "=a" (res) \
		1657	: "0" (nr), "r" (r1), "r" (r2), "r" (r3), "r" (r4), "r" (r5) \
		1658	: "cc", "r11", "cx", "memory"); \
		1659	errno = -res; \
		1660	res; \
		1661	})
		1662
		1663	#endif
		1664
		1665	#ifdef ev_syscall
		1666	#define ev_syscall0(nr) ev_syscall (nr, 0, 0, 0, 0, 0, 0, 0)
		1667	#define ev_syscall1(nr,arg1) ev_syscall (nr, 1, arg1, 0, 0, 0, 0, 0)
		1668	#define ev_syscall2(nr,arg1,arg2) ev_syscall (nr, 2, arg1, arg2, 0, 0, 0, 0)
		1669	#define ev_syscall3(nr,arg1,arg2,arg3) ev_syscall (nr, 3, arg1, arg2, arg3, 0, 0, 0)
		1670	#define ev_syscall4(nr,arg1,arg2,arg3,arg4) ev_syscall (nr, 3, arg1, arg2, arg3, arg4, 0, 0)
		1671	#define ev_syscall5(nr,arg1,arg2,arg3,arg4,arg5) ev_syscall (nr, 5, arg1, arg2, arg3, arg4, arg5, 0)
		1672	#define ev_syscall6(nr,arg1,arg2,arg3,arg4,arg5,arg6) ev_syscall (nr, 6, arg1, arg2, arg3, arg4, arg5,arg6)
		1673	#else
		1674	#define ev_syscall0(nr) syscall (nr)
		1675	#define ev_syscall1(nr,arg1) syscall (nr, arg1)
		1676	#define ev_syscall2(nr,arg1,arg2) syscall (nr, arg1, arg2)
		1677	#define ev_syscall3(nr,arg1,arg2,arg3) syscall (nr, arg1, arg2, arg3)
		1678	#define ev_syscall4(nr,arg1,arg2,arg3,arg4) syscall (nr, arg1, arg2, arg3, arg4)
		1679	#define ev_syscall5(nr,arg1,arg2,arg3,arg4,arg5) syscall (nr, arg1, arg2, arg3, arg4, arg5)
		1680	#define ev_syscall6(nr,arg1,arg2,arg3,arg4,arg5,arg6) syscall (nr, arg1, arg2, arg3, arg4, arg5,arg6)
		1681	#endif
		1682
		1683	#endif
		1684
		1685	/*****************************************************************************/
1272		1686
1273	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)	1687	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)
1274		1688
1275	#if EV_MINPRI == EV_MAXPRI	1689	#if EV_MINPRI == EV_MAXPRI
1276	# define ABSPRI(w) (((W)w), 0)	1690	# define ABSPRI(w) (((W)w), 0)
1277	#else	1691	#else
1278	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)	1692	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)
1279	#endif	1693	#endif
1280		1694
1281	#define EMPTY /* required for microsofts broken pseudo-c compiler */	1695	#define EMPTY /* required for microsofts broken pseudo-c compiler */
1282	#define EMPTY2(a,b) /* used to suppress some warnings */
1283		1696
1284	typedef ev_watcher *W;	1697	typedef ev_watcher *W;
1285	typedef ev_watcher_list *WL;	1698	typedef ev_watcher_list *WL;
1286	typedef ev_watcher_time *WT;	1699	typedef ev_watcher_time *WT;
1287		1700
…		…
1312	# include "ev_win32.c"	1725	# include "ev_win32.c"
1313	#endif	1726	#endif
1314		1727
1315	/*****************************************************************************/	1728	/*****************************************************************************/
1316		1729
		1730	#if EV_USE_LINUXAIO
		1731	# include <linux/aio_abi.h> /* probably only needed for aio_context_t */
		1732	#endif
		1733
1317	/* define a suitable floor function (only used by periodics atm) */	1734	/* define a suitable floor function (only used by periodics atm) */
1318		1735
1319	#if EV_USE_FLOOR	1736	#if EV_USE_FLOOR
1320	# include <math.h>	1737	# include <math.h>
1321	# define ev_floor(v) floor (v)	1738	# define ev_floor(v) floor (v)
1322	#else	1739	#else
1323		1740
1324	#include <float.h>	1741	#include <float.h>
1325		1742
1326	/* a floor() replacement function, should be independent of ev_tstamp type */	1743	/* a floor() replacement function, should be independent of ev_tstamp type */
		1744	ecb_noinline
1327	static ev_tstamp noinline	1745	static ev_tstamp
1328	ev_floor (ev_tstamp v)	1746	ev_floor (ev_tstamp v)
1329	{	1747	{
1330	/* the choice of shift factor is not terribly important */	1748	/* the choice of shift factor is not terribly important */
1331	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */	1749	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */
1332	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;	1750	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;
1333	#else	1751	#else
1334	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;	1752	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;
1335	#endif	1753	#endif
1336		1754
		1755	/* special treatment for negative arguments */
		1756	if (ecb_expect_false (v < 0.))
		1757	{
		1758	ev_tstamp f = -ev_floor (-v);
		1759
		1760	return f - (f == v ? 0 : 1);
		1761	}
		1762
1337	/* argument too large for an unsigned long? */	1763	/* argument too large for an unsigned long? then reduce it */
1338	if (expect_false (v >= shift))	1764	if (ecb_expect_false (v >= shift))
1339	{	1765	{
1340	ev_tstamp f;	1766	ev_tstamp f;
1341		1767
1342	if (v == v - 1.)	1768	if (v == v - 1.)
1343	return v; /* very large number */	1769	return v; /* very large numbers are assumed to be integer */
1344		1770
1345	f = shift * ev_floor (v * (1. / shift));	1771	f = shift * ev_floor (v * (1. / shift));
1346	return f + ev_floor (v - f);	1772	return f + ev_floor (v - f);
1347	}	1773	}
1348		1774
1349	/* special treatment for negative args? */
1350	if (expect_false (v < 0.))
1351	{
1352	ev_tstamp f = -ev_floor (-v);
1353
1354	return f - (f == v ? 0 : 1);
1355	}
1356
1357	/* fits into an unsigned long */	1775	/* fits into an unsigned long */
1358	return (unsigned long)v;	1776	return (unsigned long)v;
1359	}	1777	}
1360		1778
1361	#endif	1779	#endif
…		…
1364		1782
1365	#ifdef __linux	1783	#ifdef __linux
1366	# include <sys/utsname.h>	1784	# include <sys/utsname.h>
1367	#endif	1785	#endif
1368		1786
1369	static unsigned int noinline ecb_cold	1787	ecb_noinline ecb_cold
		1788	static unsigned int
1370	ev_linux_version (void)	1789	ev_linux_version (void)
1371	{	1790	{
1372	#ifdef __linux	1791	#ifdef __linux
1373	unsigned int v = 0;	1792	unsigned int v = 0;
1374	struct utsname buf;	1793	struct utsname buf;
…		…
1403	}	1822	}
1404		1823
1405	/*****************************************************************************/	1824	/*****************************************************************************/
1406		1825
1407	#if EV_AVOID_STDIO	1826	#if EV_AVOID_STDIO
1408	static void noinline ecb_cold	1827	ecb_noinline ecb_cold
		1828	static void
1409	ev_printerr (const char *msg)	1829	ev_printerr (const char *msg)
1410	{	1830	{
1411	write (STDERR_FILENO, msg, strlen (msg));	1831	write (STDERR_FILENO, msg, strlen (msg));
1412	}	1832	}
1413	#endif	1833	#endif
1414		1834
1415	static void (*syserr_cb)(const char *msg) EV_THROW;	1835	static void (*syserr_cb)(const char *msg) EV_NOEXCEPT;
1416		1836
1417	void ecb_cold	1837	ecb_cold
		1838	void
1418	ev_set_syserr_cb (void (*cb)(const char *msg) EV_THROW) EV_THROW	1839	ev_set_syserr_cb (void (*cb)(const char *msg) EV_NOEXCEPT) EV_NOEXCEPT
1419	{	1840	{
1420	syserr_cb = cb;	1841	syserr_cb = cb;
1421	}	1842	}
1422		1843
1423	static void noinline ecb_cold	1844	ecb_noinline ecb_cold
		1845	static void
1424	ev_syserr (const char *msg)	1846	ev_syserr (const char *msg)
1425	{	1847	{
1426	if (!msg)	1848	if (!msg)
1427	msg = "(libev) system error";	1849	msg = "(libev) system error";
1428		1850
…		…
1441	abort ();	1863	abort ();
1442	}	1864	}
1443	}	1865	}
1444		1866
1445	static void *	1867	static void *
1446	ev_realloc_emul (void *ptr, long size) EV_THROW	1868	ev_realloc_emul (void *ptr, long size) EV_NOEXCEPT
1447	{	1869	{
1448	/* some systems, notably openbsd and darwin, fail to properly	1870	/* some systems, notably openbsd and darwin, fail to properly
1449	* implement realloc (x, 0) (as required by both ansi c-89 and	1871	* implement realloc (x, 0) (as required by both ansi c-89 and
1450	* the single unix specification, so work around them here.	1872	* the single unix specification, so work around them here.
1451	* recently, also (at least) fedora and debian started breaking it,	1873	* recently, also (at least) fedora and debian started breaking it,
…		…
1457		1879
1458	free (ptr);	1880	free (ptr);
1459	return 0;	1881	return 0;
1460	}	1882	}
1461		1883
1462	static void *(*alloc)(void *ptr, long size) EV_THROW = ev_realloc_emul;	1884	static void *(*alloc)(void *ptr, long size) EV_NOEXCEPT = ev_realloc_emul;
1463		1885
1464	void ecb_cold	1886	ecb_cold
		1887	void
1465	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_THROW) EV_THROW	1888	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_NOEXCEPT) EV_NOEXCEPT
1466	{	1889	{
1467	alloc = cb;	1890	alloc = cb;
1468	}	1891	}
1469		1892
1470	inline_speed void *	1893	inline_speed void *
…		…
1497	typedef struct	1920	typedef struct
1498	{	1921	{
1499	WL head;	1922	WL head;
1500	unsigned char events; /* the events watched for */	1923	unsigned char events; /* the events watched for */
1501	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */	1924	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */
1502	unsigned char emask; /* the epoll backend stores the actual kernel mask in here */	1925	unsigned char emask; /* some backends store the actual kernel mask in here */
1503	unsigned char unused;	1926	unsigned char eflags; /* flags field for use by backends */
1504	#if EV_USE_EPOLL	1927	#if EV_USE_EPOLL
1505	unsigned int egen; /* generation counter to counter epoll bugs */	1928	unsigned int egen; /* generation counter to counter epoll bugs */
1506	#endif	1929	#endif
1507	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP	1930	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP
1508	SOCKET handle;	1931	SOCKET handle;
…		…
1562	static struct ev_loop default_loop_struct;	1985	static struct ev_loop default_loop_struct;
1563	EV_API_DECL struct ev_loop *ev_default_loop_ptr = 0; /* needs to be initialised to make it a definition despite extern */	1986	EV_API_DECL struct ev_loop *ev_default_loop_ptr = 0; /* needs to be initialised to make it a definition despite extern */
1564		1987
1565	#else	1988	#else
1566		1989
1567	EV_API_DECL ev_tstamp ev_rt_now = 0; /* needs to be initialised to make it a definition despite extern */	1990	EV_API_DECL ev_tstamp ev_rt_now = EV_TS_CONST (0.); /* needs to be initialised to make it a definition despite extern */
1568	#define VAR(name,decl) static decl;	1991	#define VAR(name,decl) static decl;
1569	#include "ev_vars.h"	1992	#include "ev_vars.h"
1570	#undef VAR	1993	#undef VAR
1571		1994
1572	static int ev_default_loop_ptr;	1995	static int ev_default_loop_ptr;
1573		1996
1574	#endif	1997	#endif
1575		1998
1576	#if EV_FEATURE_API	1999	#if EV_FEATURE_API
1577	# define EV_RELEASE_CB if (expect_false (release_cb)) release_cb (EV_A)	2000	# define EV_RELEASE_CB if (ecb_expect_false (release_cb)) release_cb (EV_A)
1578	# define EV_ACQUIRE_CB if (expect_false (acquire_cb)) acquire_cb (EV_A)	2001	# define EV_ACQUIRE_CB if (ecb_expect_false (acquire_cb)) acquire_cb (EV_A)
1579	# define EV_INVOKE_PENDING invoke_cb (EV_A)	2002	# define EV_INVOKE_PENDING invoke_cb (EV_A)
1580	#else	2003	#else
1581	# define EV_RELEASE_CB (void)0	2004	# define EV_RELEASE_CB (void)0
1582	# define EV_ACQUIRE_CB (void)0	2005	# define EV_ACQUIRE_CB (void)0
1583	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)	2006	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)
…		…
1587		2010
1588	/*****************************************************************************/	2011	/*****************************************************************************/
1589		2012
1590	#ifndef EV_HAVE_EV_TIME	2013	#ifndef EV_HAVE_EV_TIME
1591	ev_tstamp	2014	ev_tstamp
1592	ev_time (void) EV_THROW	2015	ev_time (void) EV_NOEXCEPT
1593	{	2016	{
1594	#if EV_USE_REALTIME	2017	#if EV_USE_REALTIME
1595	if (expect_true (have_realtime))	2018	if (ecb_expect_true (have_realtime))
1596	{	2019	{
1597	struct timespec ts;	2020	struct timespec ts;
1598	clock_gettime (CLOCK_REALTIME, &ts);	2021	clock_gettime (CLOCK_REALTIME, &ts);
1599	return ts.tv_sec + ts.tv_nsec * 1e-9;	2022	return EV_TS_GET (ts);
1600	}	2023	}
1601	#endif	2024	#endif
1602		2025
		2026	{
1603	struct timeval tv;	2027	struct timeval tv;
1604	gettimeofday (&tv, 0);	2028	gettimeofday (&tv, 0);
1605	return tv.tv_sec + tv.tv_usec * 1e-6;	2029	return EV_TV_GET (tv);
		2030	}
1606	}	2031	}
1607	#endif	2032	#endif
1608		2033
1609	inline_size ev_tstamp	2034	inline_size ev_tstamp
1610	get_clock (void)	2035	get_clock (void)
1611	{	2036	{
1612	#if EV_USE_MONOTONIC	2037	#if EV_USE_MONOTONIC
1613	if (expect_true (have_monotonic))	2038	if (ecb_expect_true (have_monotonic))
1614	{	2039	{
1615	struct timespec ts;	2040	struct timespec ts;
1616	clock_gettime (CLOCK_MONOTONIC, &ts);	2041	clock_gettime (CLOCK_MONOTONIC, &ts);
1617	return ts.tv_sec + ts.tv_nsec * 1e-9;	2042	return EV_TS_GET (ts);
1618	}	2043	}
1619	#endif	2044	#endif
1620		2045
1621	return ev_time ();	2046	return ev_time ();
1622	}	2047	}
1623		2048
1624	#if EV_MULTIPLICITY	2049	#if EV_MULTIPLICITY
1625	ev_tstamp	2050	ev_tstamp
1626	ev_now (EV_P) EV_THROW	2051	ev_now (EV_P) EV_NOEXCEPT
1627	{	2052	{
1628	return ev_rt_now;	2053	return ev_rt_now;
1629	}	2054	}
1630	#endif	2055	#endif
1631		2056
1632	void	2057	void
1633	ev_sleep (ev_tstamp delay) EV_THROW	2058	ev_sleep (ev_tstamp delay) EV_NOEXCEPT
1634	{	2059	{
1635	if (delay > 0.)	2060	if (delay > EV_TS_CONST (0.))
1636	{	2061	{
1637	#if EV_USE_NANOSLEEP	2062	#if EV_USE_NANOSLEEP
1638	struct timespec ts;	2063	struct timespec ts;
1639		2064
1640	EV_TS_SET (ts, delay);	2065	EV_TS_SET (ts, delay);
1641	nanosleep (&ts, 0);	2066	nanosleep (&ts, 0);
1642	#elif defined _WIN32	2067	#elif defined _WIN32
		2068	/* maybe this should round up, as ms is very low resolution */
		2069	/* compared to select (µs) or nanosleep (ns) */
1643	Sleep ((unsigned long)(delay * 1e3));	2070	Sleep ((unsigned long)(EV_TS_TO_MSEC (delay)));
1644	#else	2071	#else
1645	struct timeval tv;	2072	struct timeval tv;
1646		2073
1647	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */	2074	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */
1648	/* something not guaranteed by newer posix versions, but guaranteed */	2075	/* something not guaranteed by newer posix versions, but guaranteed */
…		…
1678	}	2105	}
1679		2106
1680	return ncur;	2107	return ncur;
1681	}	2108	}
1682		2109
1683	static void * noinline ecb_cold	2110	ecb_noinline ecb_cold
		2111	static void *
1684	array_realloc (int elem, void *base, int *cur, int cnt)	2112	array_realloc (int elem, void *base, int *cur, int cnt)
1685	{	2113	{
1686	*cur = array_nextsize (elem, *cur, cnt);	2114	*cur = array_nextsize (elem, *cur, cnt);
1687	return ev_realloc (base, elem * *cur);	2115	return ev_realloc (base, elem * *cur);
1688	}	2116	}
1689		2117
		2118	#define array_needsize_noinit(base,offset,count)
		2119
1690	#define array_init_zero(base,count) \	2120	#define array_needsize_zerofill(base,offset,count) \
1691	memset ((void *)(base), 0, sizeof (*(base)) * (count))	2121	memset ((void *)(base + offset), 0, sizeof (*(base)) * (count))
1692		2122
1693	#define array_needsize(type,base,cur,cnt,init) \	2123	#define array_needsize(type,base,cur,cnt,init) \
1694	if (expect_false ((cnt) > (cur))) \	2124	if (ecb_expect_false ((cnt) > (cur))) \
1695	{ \	2125	{ \
1696	int ecb_unused ocur_ = (cur); \	2126	ecb_unused int ocur_ = (cur); \
1697	(base) = (type *)array_realloc \	2127	(base) = (type *)array_realloc \
1698	(sizeof (type), (base), &(cur), (cnt)); \	2128	(sizeof (type), (base), &(cur), (cnt)); \
1699	init ((base) + (ocur_), (cur) - ocur_); \	2129	init ((base), ocur_, ((cur) - ocur_)); \
1700	}	2130	}
1701		2131
1702	#if 0	2132	#if 0
1703	#define array_slim(type,stem) \	2133	#define array_slim(type,stem) \
1704	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \	2134	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \
…		…
1713	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0	2143	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0
1714		2144
1715	/*****************************************************************************/	2145	/*****************************************************************************/
1716		2146
1717	/* dummy callback for pending events */	2147	/* dummy callback for pending events */
1718	static void noinline	2148	ecb_noinline
		2149	static void
1719	pendingcb (EV_P_ ev_prepare *w, int revents)	2150	pendingcb (EV_P_ ev_prepare *w, int revents)
1720	{	2151	{
1721	}	2152	}
1722		2153
1723	void noinline	2154	ecb_noinline
		2155	void
1724	ev_feed_event (EV_P_ void *w, int revents) EV_THROW	2156	ev_feed_event (EV_P_ void *w, int revents) EV_NOEXCEPT
1725	{	2157	{
1726	W w_ = (W)w;	2158	W w_ = (W)w;
1727	int pri = ABSPRI (w_);	2159	int pri = ABSPRI (w_);
1728		2160
1729	if (expect_false (w_->pending))	2161	if (ecb_expect_false (w_->pending))
1730	pendings [pri][w_->pending - 1].events |= revents;	2162	pendings [pri][w_->pending - 1].events |= revents;
1731	else	2163	else
1732	{	2164	{
1733	w_->pending = ++pendingcnt [pri];	2165	w_->pending = ++pendingcnt [pri];
1734	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, EMPTY2);	2166	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, array_needsize_noinit);
1735	pendings [pri][w_->pending - 1].w = w_;	2167	pendings [pri][w_->pending - 1].w = w_;
1736	pendings [pri][w_->pending - 1].events = revents;	2168	pendings [pri][w_->pending - 1].events = revents;
1737	}	2169	}
1738		2170
1739	pendingpri = NUMPRI - 1;	2171	pendingpri = NUMPRI - 1;
1740	}	2172	}
1741		2173
1742	inline_speed void	2174	inline_speed void
1743	feed_reverse (EV_P_ W w)	2175	feed_reverse (EV_P_ W w)
1744	{	2176	{
1745	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, EMPTY2);	2177	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, array_needsize_noinit);
1746	rfeeds [rfeedcnt++] = w;	2178	rfeeds [rfeedcnt++] = w;
1747	}	2179	}
1748		2180
1749	inline_size void	2181	inline_size void
1750	feed_reverse_done (EV_P_ int revents)	2182	feed_reverse_done (EV_P_ int revents)
…		…
1785	inline_speed void	2217	inline_speed void
1786	fd_event (EV_P_ int fd, int revents)	2218	fd_event (EV_P_ int fd, int revents)
1787	{	2219	{
1788	ANFD *anfd = anfds + fd;	2220	ANFD *anfd = anfds + fd;
1789		2221
1790	if (expect_true (!anfd->reify))	2222	if (ecb_expect_true (!anfd->reify))
1791	fd_event_nocheck (EV_A_ fd, revents);	2223	fd_event_nocheck (EV_A_ fd, revents);
1792	}	2224	}
1793		2225
1794	void	2226	void
1795	ev_feed_fd_event (EV_P_ int fd, int revents) EV_THROW	2227	ev_feed_fd_event (EV_P_ int fd, int revents) EV_NOEXCEPT
1796	{	2228	{
1797	if (fd >= 0 && fd < anfdmax)	2229	if (fd >= 0 && fd < anfdmax)
1798	fd_event_nocheck (EV_A_ fd, revents);	2230	fd_event_nocheck (EV_A_ fd, revents);
1799	}	2231	}
1800		2232
…		…
1837	ev_io *w;	2269	ev_io *w;
1838		2270
1839	unsigned char o_events = anfd->events;	2271	unsigned char o_events = anfd->events;
1840	unsigned char o_reify = anfd->reify;	2272	unsigned char o_reify = anfd->reify;
1841		2273
1842	anfd->reify = 0;	2274	anfd->reify = 0;
1843		2275
1844	/*if (expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */	2276	/*if (ecb_expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */
1845	{	2277	{
1846	anfd->events = 0;	2278	anfd->events = 0;
1847		2279
1848	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)	2280	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)
1849	anfd->events |= (unsigned char)w->events;	2281	anfd->events |= (unsigned char)w->events;
…		…
1858		2290
1859	fdchangecnt = 0;	2291	fdchangecnt = 0;
1860	}	2292	}
1861		2293
1862	/* something about the given fd changed */	2294	/* something about the given fd changed */
1863	inline_size void	2295	inline_size
		2296	void
1864	fd_change (EV_P_ int fd, int flags)	2297	fd_change (EV_P_ int fd, int flags)
1865	{	2298	{
1866	unsigned char reify = anfds [fd].reify;	2299	unsigned char reify = anfds [fd].reify;
1867	anfds [fd].reify |= flags;	2300	anfds [fd].reify |= flags;
1868		2301
1869	if (expect_true (!reify))	2302	if (ecb_expect_true (!reify))
1870	{	2303	{
1871	++fdchangecnt;	2304	++fdchangecnt;
1872	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, EMPTY2);	2305	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, array_needsize_noinit);
1873	fdchanges [fdchangecnt - 1] = fd;	2306	fdchanges [fdchangecnt - 1] = fd;
1874	}	2307	}
1875	}	2308	}
1876		2309
1877	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */	2310	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */
1878	inline_speed void ecb_cold	2311	inline_speed ecb_cold void
1879	fd_kill (EV_P_ int fd)	2312	fd_kill (EV_P_ int fd)
1880	{	2313	{
1881	ev_io *w;	2314	ev_io *w;
1882		2315
1883	while ((w = (ev_io *)anfds [fd].head))	2316	while ((w = (ev_io *)anfds [fd].head))
…		…
1886	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);	2319	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);
1887	}	2320	}
1888	}	2321	}
1889		2322
1890	/* check whether the given fd is actually valid, for error recovery */	2323	/* check whether the given fd is actually valid, for error recovery */
1891	inline_size int ecb_cold	2324	inline_size ecb_cold int
1892	fd_valid (int fd)	2325	fd_valid (int fd)
1893	{	2326	{
1894	#ifdef _WIN32	2327	#ifdef _WIN32
1895	return EV_FD_TO_WIN32_HANDLE (fd) != -1;	2328	return EV_FD_TO_WIN32_HANDLE (fd) != -1;
1896	#else	2329	#else
1897	return fcntl (fd, F_GETFD) != -1;	2330	return fcntl (fd, F_GETFD) != -1;
1898	#endif	2331	#endif
1899	}	2332	}
1900		2333
1901	/* called on EBADF to verify fds */	2334	/* called on EBADF to verify fds */
1902	static void noinline ecb_cold	2335	ecb_noinline ecb_cold
		2336	static void
1903	fd_ebadf (EV_P)	2337	fd_ebadf (EV_P)
1904	{	2338	{
1905	int fd;	2339	int fd;
1906		2340
1907	for (fd = 0; fd < anfdmax; ++fd)	2341	for (fd = 0; fd < anfdmax; ++fd)
…		…
1909	if (!fd_valid (fd) && errno == EBADF)	2343	if (!fd_valid (fd) && errno == EBADF)
1910	fd_kill (EV_A_ fd);	2344	fd_kill (EV_A_ fd);
1911	}	2345	}
1912		2346
1913	/* called on ENOMEM in select/poll to kill some fds and retry */	2347	/* called on ENOMEM in select/poll to kill some fds and retry */
1914	static void noinline ecb_cold	2348	ecb_noinline ecb_cold
		2349	static void
1915	fd_enomem (EV_P)	2350	fd_enomem (EV_P)
1916	{	2351	{
1917	int fd;	2352	int fd;
1918		2353
1919	for (fd = anfdmax; fd--; )	2354	for (fd = anfdmax; fd--; )
…		…
1923	break;	2358	break;
1924	}	2359	}
1925	}	2360	}
1926		2361
1927	/* usually called after fork if backend needs to re-arm all fds from scratch */	2362	/* usually called after fork if backend needs to re-arm all fds from scratch */
1928	static void noinline	2363	ecb_noinline
		2364	static void
1929	fd_rearm_all (EV_P)	2365	fd_rearm_all (EV_P)
1930	{	2366	{
1931	int fd;	2367	int fd;
1932		2368
1933	for (fd = 0; fd < anfdmax; ++fd)	2369	for (fd = 0; fd < anfdmax; ++fd)
…		…
1986	ev_tstamp minat;	2422	ev_tstamp minat;
1987	ANHE *minpos;	2423	ANHE *minpos;
1988	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;	2424	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;
1989		2425
1990	/* find minimum child */	2426	/* find minimum child */
1991	if (expect_true (pos + DHEAP - 1 < E))	2427	if (ecb_expect_true (pos + DHEAP - 1 < E))
1992	{	2428	{
1993	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));	2429	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));
1994	if ( ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));	2430	if ( minat > ANHE_at (pos [1])) (minpos = pos + 1), (minat = ANHE_at (*minpos));
1995	if ( ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));	2431	if ( minat > ANHE_at (pos [2])) (minpos = pos + 2), (minat = ANHE_at (*minpos));
1996	if ( ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));	2432	if ( minat > ANHE_at (pos [3])) (minpos = pos + 3), (minat = ANHE_at (*minpos));
1997	}	2433	}
1998	else if (pos < E)	2434	else if (pos < E)
1999	{	2435	{
2000	/* slow path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));	2436	/* slow path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));
2001	if (pos + 1 < E && ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));	2437	if (pos + 1 < E && minat > ANHE_at (pos [1])) (minpos = pos + 1), (minat = ANHE_at (*minpos));
2002	if (pos + 2 < E && ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));	2438	if (pos + 2 < E && minat > ANHE_at (pos [2])) (minpos = pos + 2), (minat = ANHE_at (*minpos));
2003	if (pos + 3 < E && ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));	2439	if (pos + 3 < E && minat > ANHE_at (pos [3])) (minpos = pos + 3), (minat = ANHE_at (*minpos));
2004	}	2440	}
2005	else	2441	else
2006	break;	2442	break;
2007		2443
2008	if (ANHE_at (he) <= minat)	2444	if (ANHE_at (he) <= minat)
…		…
2016		2452
2017	heap [k] = he;	2453	heap [k] = he;
2018	ev_active (ANHE_w (he)) = k;	2454	ev_active (ANHE_w (he)) = k;
2019	}	2455	}
2020		2456
2021	#else /* 4HEAP */	2457	#else /* not 4HEAP */
2022		2458
2023	#define HEAP0 1	2459	#define HEAP0 1
2024	#define HPARENT(k) ((k) >> 1)	2460	#define HPARENT(k) ((k) >> 1)
2025	#define UPHEAP_DONE(p,k) (!(p))	2461	#define UPHEAP_DONE(p,k) (!(p))
2026		2462
…		…
2114		2550
2115	/*****************************************************************************/	2551	/*****************************************************************************/
2116		2552
2117	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	2553	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2118		2554
2119	static void noinline ecb_cold	2555	ecb_noinline ecb_cold
		2556	static void
2120	evpipe_init (EV_P)	2557	evpipe_init (EV_P)
2121	{	2558	{
2122	if (!ev_is_active (&pipe_w))	2559	if (!ev_is_active (&pipe_w))
2123	{	2560	{
2124	int fds [2];	2561	int fds [2];
…		…
2164	inline_speed void	2601	inline_speed void
2165	evpipe_write (EV_P_ EV_ATOMIC_T *flag)	2602	evpipe_write (EV_P_ EV_ATOMIC_T *flag)
2166	{	2603	{
2167	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */	2604	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */
2168		2605
2169	if (expect_true (*flag))	2606	if (ecb_expect_true (*flag))
2170	return;	2607	return;
2171		2608
2172	*flag = 1;	2609	*flag = 1;
2173	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */	2610	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */
2174		2611
…		…
2195	#endif	2632	#endif
2196	{	2633	{
2197	#ifdef _WIN32	2634	#ifdef _WIN32
2198	WSABUF buf;	2635	WSABUF buf;
2199	DWORD sent;	2636	DWORD sent;
2200	buf.buf = &buf;	2637	buf.buf = (char *)&buf;
2201	buf.len = 1;	2638	buf.len = 1;
2202	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);	2639	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);
2203	#else	2640	#else
2204	write (evpipe [1], &(evpipe [1]), 1);	2641	write (evpipe [1], &(evpipe [1]), 1);
2205	#endif	2642	#endif
…		…
2251	sig_pending = 0;	2688	sig_pending = 0;
2252		2689
2253	ECB_MEMORY_FENCE;	2690	ECB_MEMORY_FENCE;
2254		2691
2255	for (i = EV_NSIG - 1; i--; )	2692	for (i = EV_NSIG - 1; i--; )
2256	if (expect_false (signals [i].pending))	2693	if (ecb_expect_false (signals [i].pending))
2257	ev_feed_signal_event (EV_A_ i + 1);	2694	ev_feed_signal_event (EV_A_ i + 1);
2258	}	2695	}
2259	#endif	2696	#endif
2260		2697
2261	#if EV_ASYNC_ENABLE	2698	#if EV_ASYNC_ENABLE
…		…
2277	}	2714	}
2278		2715
2279	/*****************************************************************************/	2716	/*****************************************************************************/
2280		2717
2281	void	2718	void
2282	ev_feed_signal (int signum) EV_THROW	2719	ev_feed_signal (int signum) EV_NOEXCEPT
2283	{	2720	{
2284	#if EV_MULTIPLICITY	2721	#if EV_MULTIPLICITY
2285	EV_P;	2722	EV_P;
2286	ECB_MEMORY_FENCE_ACQUIRE;	2723	ECB_MEMORY_FENCE_ACQUIRE;
2287	EV_A = signals [signum - 1].loop;	2724	EV_A = signals [signum - 1].loop;
…		…
2302	#endif	2739	#endif
2303		2740
2304	ev_feed_signal (signum);	2741	ev_feed_signal (signum);
2305	}	2742	}
2306		2743
2307	void noinline	2744	ecb_noinline
		2745	void
2308	ev_feed_signal_event (EV_P_ int signum) EV_THROW	2746	ev_feed_signal_event (EV_P_ int signum) EV_NOEXCEPT
2309	{	2747	{
2310	WL w;	2748	WL w;
2311		2749
2312	if (expect_false (signum <= 0 || signum >= EV_NSIG))	2750	if (ecb_expect_false (signum <= 0 || signum >= EV_NSIG))
2313	return;	2751	return;
2314		2752
2315	--signum;	2753	--signum;
2316		2754
2317	#if EV_MULTIPLICITY	2755	#if EV_MULTIPLICITY
2318	/* it is permissible to try to feed a signal to the wrong loop */	2756	/* it is permissible to try to feed a signal to the wrong loop */
2319	/* or, likely more useful, feeding a signal nobody is waiting for */	2757	/* or, likely more useful, feeding a signal nobody is waiting for */
2320		2758
2321	if (expect_false (signals [signum].loop != EV_A))	2759	if (ecb_expect_false (signals [signum].loop != EV_A))
2322	return;	2760	return;
2323	#endif	2761	#endif
2324		2762
2325	signals [signum].pending = 0;	2763	signals [signum].pending = 0;
2326	ECB_MEMORY_FENCE_RELEASE;	2764	ECB_MEMORY_FENCE_RELEASE;
…		…
2422	# include "ev_kqueue.c"	2860	# include "ev_kqueue.c"
2423	#endif	2861	#endif
2424	#if EV_USE_EPOLL	2862	#if EV_USE_EPOLL
2425	# include "ev_epoll.c"	2863	# include "ev_epoll.c"
2426	#endif	2864	#endif
		2865	#if EV_USE_LINUXAIO
		2866	# include "ev_linuxaio.c"
		2867	#endif
		2868	#if EV_USE_IOURING
		2869	# include "ev_iouring.c"
		2870	#endif
2427	#if EV_USE_POLL	2871	#if EV_USE_POLL
2428	# include "ev_poll.c"	2872	# include "ev_poll.c"
2429	#endif	2873	#endif
2430	#if EV_USE_SELECT	2874	#if EV_USE_SELECT
2431	# include "ev_select.c"	2875	# include "ev_select.c"
2432	#endif	2876	#endif
2433		2877
2434	int ecb_cold	2878	ecb_cold int
2435	ev_version_major (void) EV_THROW	2879	ev_version_major (void) EV_NOEXCEPT
2436	{	2880	{
2437	return EV_VERSION_MAJOR;	2881	return EV_VERSION_MAJOR;
2438	}	2882	}
2439		2883
2440	int ecb_cold	2884	ecb_cold int
2441	ev_version_minor (void) EV_THROW	2885	ev_version_minor (void) EV_NOEXCEPT
2442	{	2886	{
2443	return EV_VERSION_MINOR;	2887	return EV_VERSION_MINOR;
2444	}	2888	}
2445		2889
2446	/* return true if we are running with elevated privileges and should ignore env variables */	2890	/* return true if we are running with elevated privileges and should ignore env variables */
2447	int inline_size ecb_cold	2891	inline_size ecb_cold int
2448	enable_secure (void)	2892	enable_secure (void)
2449	{	2893	{
2450	#ifdef _WIN32	2894	#ifdef _WIN32
2451	return 0;	2895	return 0;
2452	#else	2896	#else
2453	return getuid () != geteuid ()	2897	return getuid () != geteuid ()
2454	|| getgid () != getegid ();	2898	|| getgid () != getegid ();
2455	#endif	2899	#endif
2456	}	2900	}
2457		2901
2458	unsigned int ecb_cold	2902	ecb_cold
		2903	unsigned int
2459	ev_supported_backends (void) EV_THROW	2904	ev_supported_backends (void) EV_NOEXCEPT
2460	{	2905	{
2461	unsigned int flags = 0;	2906	unsigned int flags = 0;
2462		2907
2463	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;	2908	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;
2464	if (EV_USE_KQUEUE) flags |= EVBACKEND_KQUEUE;	2909	if (EV_USE_KQUEUE ) flags |= EVBACKEND_KQUEUE;
2465	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;	2910	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;
		2911	if (EV_USE_LINUXAIO) flags |= EVBACKEND_LINUXAIO;
		2912	if (EV_USE_IOURING ) flags |= EVBACKEND_IOURING;
2466	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;	2913	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;
2467	if (EV_USE_SELECT) flags |= EVBACKEND_SELECT;	2914	if (EV_USE_SELECT ) flags |= EVBACKEND_SELECT;
2468		2915
2469	return flags;	2916	return flags;
2470	}	2917	}
2471		2918
2472	unsigned int ecb_cold	2919	ecb_cold
		2920	unsigned int
2473	ev_recommended_backends (void) EV_THROW	2921	ev_recommended_backends (void) EV_NOEXCEPT
2474	{	2922	{
2475	unsigned int flags = ev_supported_backends ();	2923	unsigned int flags = ev_supported_backends ();
2476		2924
2477	#ifndef __NetBSD__	2925	#ifndef __NetBSD__
2478	/* kqueue is borked on everything but netbsd apparently */	2926	/* kqueue is borked on everything but netbsd apparently */
…		…
2486	#endif	2934	#endif
2487	#ifdef __FreeBSD__	2935	#ifdef __FreeBSD__
2488	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */	2936	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */
2489	#endif	2937	#endif
2490		2938
		2939	/* TODO: linuxaio is very experimental */
		2940	#if !EV_RECOMMEND_LINUXAIO
		2941	flags &= ~EVBACKEND_LINUXAIO;
		2942	#endif
		2943	/* TODO: linuxaio is super experimental */
		2944	#if !EV_RECOMMEND_IOURING
		2945	flags &= ~EVBACKEND_IOURING;
		2946	#endif
		2947
2491	return flags;	2948	return flags;
2492	}	2949	}
2493		2950
2494	unsigned int ecb_cold	2951	ecb_cold
		2952	unsigned int
2495	ev_embeddable_backends (void) EV_THROW	2953	ev_embeddable_backends (void) EV_NOEXCEPT
2496	{	2954	{
2497	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;	2955	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;
2498		2956
2499	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */	2957	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */
2500	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */	2958	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */
2501	flags &= ~EVBACKEND_EPOLL;	2959	flags &= ~EVBACKEND_EPOLL;
2502		2960
		2961	/* EVBACKEND_LINUXAIO is theoretically embeddable, but suffers from a performance overhead */
		2962
		2963	/* EVBACKEND_IOURING is practically embeddable, but the current implementation is not
		2964	* because our backend_fd is the epoll fd we need as fallback.
		2965	* if the kernel ever is fixed, this might change...
		2966	*/
		2967
2503	return flags;	2968	return flags;
2504	}	2969	}
2505		2970
2506	unsigned int	2971	unsigned int
2507	ev_backend (EV_P) EV_THROW	2972	ev_backend (EV_P) EV_NOEXCEPT
2508	{	2973	{
2509	return backend;	2974	return backend;
2510	}	2975	}
2511		2976
2512	#if EV_FEATURE_API	2977	#if EV_FEATURE_API
2513	unsigned int	2978	unsigned int
2514	ev_iteration (EV_P) EV_THROW	2979	ev_iteration (EV_P) EV_NOEXCEPT
2515	{	2980	{
2516	return loop_count;	2981	return loop_count;
2517	}	2982	}
2518		2983
2519	unsigned int	2984	unsigned int
2520	ev_depth (EV_P) EV_THROW	2985	ev_depth (EV_P) EV_NOEXCEPT
2521	{	2986	{
2522	return loop_depth;	2987	return loop_depth;
2523	}	2988	}
2524		2989
2525	void	2990	void
2526	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2991	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2527	{	2992	{
2528	io_blocktime = interval;	2993	io_blocktime = interval;
2529	}	2994	}
2530		2995
2531	void	2996	void
2532	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2997	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2533	{	2998	{
2534	timeout_blocktime = interval;	2999	timeout_blocktime = interval;
2535	}	3000	}
2536		3001
2537	void	3002	void
2538	ev_set_userdata (EV_P_ void *data) EV_THROW	3003	ev_set_userdata (EV_P_ void *data) EV_NOEXCEPT
2539	{	3004	{
2540	userdata = data;	3005	userdata = data;
2541	}	3006	}
2542		3007
2543	void *	3008	void *
2544	ev_userdata (EV_P) EV_THROW	3009	ev_userdata (EV_P) EV_NOEXCEPT
2545	{	3010	{
2546	return userdata;	3011	return userdata;
2547	}	3012	}
2548		3013
2549	void	3014	void
2550	ev_set_invoke_pending_cb (EV_P_ void (*invoke_pending_cb)(EV_P)) EV_THROW	3015	ev_set_invoke_pending_cb (EV_P_ ev_loop_callback invoke_pending_cb) EV_NOEXCEPT
2551	{	3016	{
2552	invoke_cb = invoke_pending_cb;	3017	invoke_cb = invoke_pending_cb;
2553	}	3018	}
2554		3019
2555	void	3020	void
2556	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_THROW, void (*acquire)(EV_P) EV_THROW) EV_THROW	3021	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_NOEXCEPT, void (*acquire)(EV_P) EV_NOEXCEPT) EV_NOEXCEPT
2557	{	3022	{
2558	release_cb = release;	3023	release_cb = release;
2559	acquire_cb = acquire;	3024	acquire_cb = acquire;
2560	}	3025	}
2561	#endif	3026	#endif
2562		3027
2563	/* initialise a loop structure, must be zero-initialised */	3028	/* initialise a loop structure, must be zero-initialised */
2564	static void noinline ecb_cold	3029	ecb_noinline ecb_cold
		3030	static void
2565	loop_init (EV_P_ unsigned int flags) EV_THROW	3031	loop_init (EV_P_ unsigned int flags) EV_NOEXCEPT
2566	{	3032	{
2567	if (!backend)	3033	if (!backend)
2568	{	3034	{
2569	origflags = flags;	3035	origflags = flags;
2570		3036
…		…
2628		3094
2629	if (!(flags & EVBACKEND_MASK))	3095	if (!(flags & EVBACKEND_MASK))
2630	flags |= ev_recommended_backends ();	3096	flags |= ev_recommended_backends ();
2631		3097
2632	#if EV_USE_IOCP	3098	#if EV_USE_IOCP
2633	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);	3099	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);
2634	#endif	3100	#endif
2635	#if EV_USE_PORT	3101	#if EV_USE_PORT
2636	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);	3102	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);
2637	#endif	3103	#endif
2638	#if EV_USE_KQUEUE	3104	#if EV_USE_KQUEUE
2639	if (!backend && (flags & EVBACKEND_KQUEUE)) backend = kqueue_init (EV_A_ flags);	3105	if (!backend && (flags & EVBACKEND_KQUEUE )) backend = kqueue_init (EV_A_ flags);
		3106	#endif
		3107	#if EV_USE_IOURING
		3108	if (!backend && (flags & EVBACKEND_IOURING )) backend = iouring_init (EV_A_ flags);
		3109	#endif
		3110	#if EV_USE_LINUXAIO
		3111	if (!backend && (flags & EVBACKEND_LINUXAIO)) backend = linuxaio_init (EV_A_ flags);
2640	#endif	3112	#endif
2641	#if EV_USE_EPOLL	3113	#if EV_USE_EPOLL
2642	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);	3114	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);
2643	#endif	3115	#endif
2644	#if EV_USE_POLL	3116	#if EV_USE_POLL
2645	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);	3117	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);
2646	#endif	3118	#endif
2647	#if EV_USE_SELECT	3119	#if EV_USE_SELECT
2648	if (!backend && (flags & EVBACKEND_SELECT)) backend = select_init (EV_A_ flags);	3120	if (!backend && (flags & EVBACKEND_SELECT )) backend = select_init (EV_A_ flags);
2649	#endif	3121	#endif
2650		3122
2651	ev_prepare_init (&pending_w, pendingcb);	3123	ev_prepare_init (&pending_w, pendingcb);
2652		3124
2653	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	3125	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
…		…
2656	#endif	3128	#endif
2657	}	3129	}
2658	}	3130	}
2659		3131
2660	/* free up a loop structure */	3132	/* free up a loop structure */
2661	void ecb_cold	3133	ecb_cold
		3134	void
2662	ev_loop_destroy (EV_P)	3135	ev_loop_destroy (EV_P)
2663	{	3136	{
2664	int i;	3137	int i;
2665		3138
2666	#if EV_MULTIPLICITY	3139	#if EV_MULTIPLICITY
…		…
2669	return;	3142	return;
2670	#endif	3143	#endif
2671		3144
2672	#if EV_CLEANUP_ENABLE	3145	#if EV_CLEANUP_ENABLE
2673	/* queue cleanup watchers (and execute them) */	3146	/* queue cleanup watchers (and execute them) */
2674	if (expect_false (cleanupcnt))	3147	if (ecb_expect_false (cleanupcnt))
2675	{	3148	{
2676	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);	3149	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);
2677	EV_INVOKE_PENDING;	3150	EV_INVOKE_PENDING;
2678	}	3151	}
2679	#endif	3152	#endif
…		…
2707		3180
2708	if (backend_fd >= 0)	3181	if (backend_fd >= 0)
2709	close (backend_fd);	3182	close (backend_fd);
2710		3183
2711	#if EV_USE_IOCP	3184	#if EV_USE_IOCP
2712	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);	3185	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);
2713	#endif	3186	#endif
2714	#if EV_USE_PORT	3187	#if EV_USE_PORT
2715	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);	3188	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);
2716	#endif	3189	#endif
2717	#if EV_USE_KQUEUE	3190	#if EV_USE_KQUEUE
2718	if (backend == EVBACKEND_KQUEUE) kqueue_destroy (EV_A);	3191	if (backend == EVBACKEND_KQUEUE ) kqueue_destroy (EV_A);
		3192	#endif
		3193	#if EV_USE_IOURING
		3194	if (backend == EVBACKEND_IOURING ) iouring_destroy (EV_A);
		3195	#endif
		3196	#if EV_USE_LINUXAIO
		3197	if (backend == EVBACKEND_LINUXAIO) linuxaio_destroy (EV_A);
2719	#endif	3198	#endif
2720	#if EV_USE_EPOLL	3199	#if EV_USE_EPOLL
2721	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);	3200	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);
2722	#endif	3201	#endif
2723	#if EV_USE_POLL	3202	#if EV_USE_POLL
2724	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);	3203	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);
2725	#endif	3204	#endif
2726	#if EV_USE_SELECT	3205	#if EV_USE_SELECT
2727	if (backend == EVBACKEND_SELECT) select_destroy (EV_A);	3206	if (backend == EVBACKEND_SELECT ) select_destroy (EV_A);
2728	#endif	3207	#endif
2729		3208
2730	for (i = NUMPRI; i--; )	3209	for (i = NUMPRI; i--; )
2731	{	3210	{
2732	array_free (pending, [i]);	3211	array_free (pending, [i]);
…		…
2774		3253
2775	inline_size void	3254	inline_size void
2776	loop_fork (EV_P)	3255	loop_fork (EV_P)
2777	{	3256	{
2778	#if EV_USE_PORT	3257	#if EV_USE_PORT
2779	if (backend == EVBACKEND_PORT ) port_fork (EV_A);	3258	if (backend == EVBACKEND_PORT ) port_fork (EV_A);
2780	#endif	3259	#endif
2781	#if EV_USE_KQUEUE	3260	#if EV_USE_KQUEUE
2782	if (backend == EVBACKEND_KQUEUE) kqueue_fork (EV_A);	3261	if (backend == EVBACKEND_KQUEUE ) kqueue_fork (EV_A);
		3262	#endif
		3263	#if EV_USE_IOURING
		3264	if (backend == EVBACKEND_IOURING ) iouring_fork (EV_A);
		3265	#endif
		3266	#if EV_USE_LINUXAIO
		3267	if (backend == EVBACKEND_LINUXAIO) linuxaio_fork (EV_A);
2783	#endif	3268	#endif
2784	#if EV_USE_EPOLL	3269	#if EV_USE_EPOLL
2785	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);	3270	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);
2786	#endif	3271	#endif
2787	#if EV_USE_INOTIFY	3272	#if EV_USE_INOTIFY
2788	infy_fork (EV_A);	3273	infy_fork (EV_A);
2789	#endif	3274	#endif
2790		3275
2791	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	3276	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2792	if (ev_is_active (&pipe_w))	3277	if (ev_is_active (&pipe_w) && postfork != 2)
2793	{	3278	{
2794	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */	3279	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */
2795		3280
2796	ev_ref (EV_A);	3281	ev_ref (EV_A);
2797	ev_io_stop (EV_A_ &pipe_w);	3282	ev_io_stop (EV_A_ &pipe_w);
…		…
2808	postfork = 0;	3293	postfork = 0;
2809	}	3294	}
2810		3295
2811	#if EV_MULTIPLICITY	3296	#if EV_MULTIPLICITY
2812		3297
		3298	ecb_cold
2813	struct ev_loop * ecb_cold	3299	struct ev_loop *
2814	ev_loop_new (unsigned int flags) EV_THROW	3300	ev_loop_new (unsigned int flags) EV_NOEXCEPT
2815	{	3301	{
2816	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));	3302	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));
2817		3303
2818	memset (EV_A, 0, sizeof (struct ev_loop));	3304	memset (EV_A, 0, sizeof (struct ev_loop));
2819	loop_init (EV_A_ flags);	3305	loop_init (EV_A_ flags);
…		…
2826	}	3312	}
2827		3313
2828	#endif /* multiplicity */	3314	#endif /* multiplicity */
2829		3315
2830	#if EV_VERIFY	3316	#if EV_VERIFY
2831	static void noinline ecb_cold	3317	ecb_noinline ecb_cold
		3318	static void
2832	verify_watcher (EV_P_ W w)	3319	verify_watcher (EV_P_ W w)
2833	{	3320	{
2834	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));	3321	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));
2835		3322
2836	if (w->pending)	3323	if (w->pending)
2837	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));	3324	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));
2838	}	3325	}
2839		3326
2840	static void noinline ecb_cold	3327	ecb_noinline ecb_cold
		3328	static void
2841	verify_heap (EV_P_ ANHE *heap, int N)	3329	verify_heap (EV_P_ ANHE *heap, int N)
2842	{	3330	{
2843	int i;	3331	int i;
2844		3332
2845	for (i = HEAP0; i < N + HEAP0; ++i)	3333	for (i = HEAP0; i < N + HEAP0; ++i)
…		…
2850		3338
2851	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));	3339	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));
2852	}	3340	}
2853	}	3341	}
2854		3342
2855	static void noinline ecb_cold	3343	ecb_noinline ecb_cold
		3344	static void
2856	array_verify (EV_P_ W *ws, int cnt)	3345	array_verify (EV_P_ W *ws, int cnt)
2857	{	3346	{
2858	while (cnt--)	3347	while (cnt--)
2859	{	3348	{
2860	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));	3349	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));
…		…
2863	}	3352	}
2864	#endif	3353	#endif
2865		3354
2866	#if EV_FEATURE_API	3355	#if EV_FEATURE_API
2867	void ecb_cold	3356	void ecb_cold
2868	ev_verify (EV_P) EV_THROW	3357	ev_verify (EV_P) EV_NOEXCEPT
2869	{	3358	{
2870	#if EV_VERIFY	3359	#if EV_VERIFY
2871	int i;	3360	int i;
2872	WL w, w2;	3361	WL w, w2;
2873		3362
…		…
2949	#endif	3438	#endif
2950	}	3439	}
2951	#endif	3440	#endif
2952		3441
2953	#if EV_MULTIPLICITY	3442	#if EV_MULTIPLICITY
		3443	ecb_cold
2954	struct ev_loop * ecb_cold	3444	struct ev_loop *
2955	#else	3445	#else
2956	int	3446	int
2957	#endif	3447	#endif
2958	ev_default_loop (unsigned int flags) EV_THROW	3448	ev_default_loop (unsigned int flags) EV_NOEXCEPT
2959	{	3449	{
2960	if (!ev_default_loop_ptr)	3450	if (!ev_default_loop_ptr)
2961	{	3451	{
2962	#if EV_MULTIPLICITY	3452	#if EV_MULTIPLICITY
2963	EV_P = ev_default_loop_ptr = &default_loop_struct;	3453	EV_P = ev_default_loop_ptr = &default_loop_struct;
…		…
2982		3472
2983	return ev_default_loop_ptr;	3473	return ev_default_loop_ptr;
2984	}	3474	}
2985		3475
2986	void	3476	void
2987	ev_loop_fork (EV_P) EV_THROW	3477	ev_loop_fork (EV_P) EV_NOEXCEPT
2988	{	3478	{
2989	postfork = 1;	3479	postfork = 1;
2990	}	3480	}
2991		3481
2992	/*****************************************************************************/	3482	/*****************************************************************************/
…		…
2996	{	3486	{
2997	EV_CB_INVOKE ((W)w, revents);	3487	EV_CB_INVOKE ((W)w, revents);
2998	}	3488	}
2999		3489
3000	unsigned int	3490	unsigned int
3001	ev_pending_count (EV_P) EV_THROW	3491	ev_pending_count (EV_P) EV_NOEXCEPT
3002	{	3492	{
3003	int pri;	3493	int pri;
3004	unsigned int count = 0;	3494	unsigned int count = 0;
3005		3495
3006	for (pri = NUMPRI; pri--; )	3496	for (pri = NUMPRI; pri--; )
3007	count += pendingcnt [pri];	3497	count += pendingcnt [pri];
3008		3498
3009	return count;	3499	return count;
3010	}	3500	}
3011		3501
3012	void noinline	3502	ecb_noinline
		3503	void
3013	ev_invoke_pending (EV_P)	3504	ev_invoke_pending (EV_P)
3014	{	3505	{
3015	pendingpri = NUMPRI;	3506	pendingpri = NUMPRI;
3016		3507
3017	while (pendingpri) /* pendingpri possibly gets modified in the inner loop */	3508	do
3018	{	3509	{
3019	--pendingpri;	3510	--pendingpri;
3020		3511
		3512	/* pendingpri possibly gets modified in the inner loop */
3021	while (pendingcnt [pendingpri])	3513	while (pendingcnt [pendingpri])
3022	{	3514	{
3023	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];	3515	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];
3024		3516
3025	p->w->pending = 0;	3517	p->w->pending = 0;
3026	EV_CB_INVOKE (p->w, p->events);	3518	EV_CB_INVOKE (p->w, p->events);
3027	EV_FREQUENT_CHECK;	3519	EV_FREQUENT_CHECK;
3028	}	3520	}
3029	}	3521	}
		3522	while (pendingpri);
3030	}	3523	}
3031		3524
3032	#if EV_IDLE_ENABLE	3525	#if EV_IDLE_ENABLE
3033	/* make idle watchers pending. this handles the "call-idle */	3526	/* make idle watchers pending. this handles the "call-idle */
3034	/* only when higher priorities are idle" logic */	3527	/* only when higher priorities are idle" logic */
3035	inline_size void	3528	inline_size void
3036	idle_reify (EV_P)	3529	idle_reify (EV_P)
3037	{	3530	{
3038	if (expect_false (idleall))	3531	if (ecb_expect_false (idleall))
3039	{	3532	{
3040	int pri;	3533	int pri;
3041		3534
3042	for (pri = NUMPRI; pri--; )	3535	for (pri = NUMPRI; pri--; )
3043	{	3536	{
…		…
3073	{	3566	{
3074	ev_at (w) += w->repeat;	3567	ev_at (w) += w->repeat;
3075	if (ev_at (w) < mn_now)	3568	if (ev_at (w) < mn_now)
3076	ev_at (w) = mn_now;	3569	ev_at (w) = mn_now;
3077		3570
3078	assert (("libev: negative ev_timer repeat value found while processing timers", w->repeat > 0.));	3571	assert (("libev: negative ev_timer repeat value found while processing timers", w->repeat > EV_TS_CONST (0.)));
3079		3572
3080	ANHE_at_cache (timers [HEAP0]);	3573	ANHE_at_cache (timers [HEAP0]);
3081	downheap (timers, timercnt, HEAP0);	3574	downheap (timers, timercnt, HEAP0);
3082	}	3575	}
3083	else	3576	else
…		…
3092	}	3585	}
3093	}	3586	}
3094		3587
3095	#if EV_PERIODIC_ENABLE	3588	#if EV_PERIODIC_ENABLE
3096		3589
3097	static void noinline	3590	ecb_noinline
		3591	static void
3098	periodic_recalc (EV_P_ ev_periodic *w)	3592	periodic_recalc (EV_P_ ev_periodic *w)
3099	{	3593	{
3100	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;	3594	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;
3101	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);	3595	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);
3102		3596
…		…
3104	while (at <= ev_rt_now)	3598	while (at <= ev_rt_now)
3105	{	3599	{
3106	ev_tstamp nat = at + w->interval;	3600	ev_tstamp nat = at + w->interval;
3107		3601
3108	/* when resolution fails us, we use ev_rt_now */	3602	/* when resolution fails us, we use ev_rt_now */
3109	if (expect_false (nat == at))	3603	if (ecb_expect_false (nat == at))
3110	{	3604	{
3111	at = ev_rt_now;	3605	at = ev_rt_now;
3112	break;	3606	break;
3113	}	3607	}
3114		3608
…		…
3160	}	3654	}
3161	}	3655	}
3162		3656
3163	/* simply recalculate all periodics */	3657	/* simply recalculate all periodics */
3164	/* TODO: maybe ensure that at least one event happens when jumping forward? */	3658	/* TODO: maybe ensure that at least one event happens when jumping forward? */
3165	static void noinline ecb_cold	3659	ecb_noinline ecb_cold
		3660	static void
3166	periodics_reschedule (EV_P)	3661	periodics_reschedule (EV_P)
3167	{	3662	{
3168	int i;	3663	int i;
3169		3664
3170	/* adjust periodics after time jump */	3665	/* adjust periodics after time jump */
…		…
3183	reheap (periodics, periodiccnt);	3678	reheap (periodics, periodiccnt);
3184	}	3679	}
3185	#endif	3680	#endif
3186		3681
3187	/* adjust all timers by a given offset */	3682	/* adjust all timers by a given offset */
3188	static void noinline ecb_cold	3683	ecb_noinline ecb_cold
		3684	static void
3189	timers_reschedule (EV_P_ ev_tstamp adjust)	3685	timers_reschedule (EV_P_ ev_tstamp adjust)
3190	{	3686	{
3191	int i;	3687	int i;
3192		3688
3193	for (i = 0; i < timercnt; ++i)	3689	for (i = 0; i < timercnt; ++i)
…		…
3202	/* also detect if there was a timejump, and act accordingly */	3698	/* also detect if there was a timejump, and act accordingly */
3203	inline_speed void	3699	inline_speed void
3204	time_update (EV_P_ ev_tstamp max_block)	3700	time_update (EV_P_ ev_tstamp max_block)
3205	{	3701	{
3206	#if EV_USE_MONOTONIC	3702	#if EV_USE_MONOTONIC
3207	if (expect_true (have_monotonic))	3703	if (ecb_expect_true (have_monotonic))
3208	{	3704	{
3209	int i;	3705	int i;
3210	ev_tstamp odiff = rtmn_diff;	3706	ev_tstamp odiff = rtmn_diff;
3211		3707
3212	mn_now = get_clock ();	3708	mn_now = get_clock ();
3213		3709
3214	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */	3710	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */
3215	/* interpolate in the meantime */	3711	/* interpolate in the meantime */
3216	if (expect_true (mn_now - now_floor < MIN_TIMEJUMP * .5))	3712	if (ecb_expect_true (mn_now - now_floor < EV_TS_CONST (MIN_TIMEJUMP * .5)))
3217	{	3713	{
3218	ev_rt_now = rtmn_diff + mn_now;	3714	ev_rt_now = rtmn_diff + mn_now;
3219	return;	3715	return;
3220	}	3716	}
3221		3717
…		…
3235	ev_tstamp diff;	3731	ev_tstamp diff;
3236	rtmn_diff = ev_rt_now - mn_now;	3732	rtmn_diff = ev_rt_now - mn_now;
3237		3733
3238	diff = odiff - rtmn_diff;	3734	diff = odiff - rtmn_diff;
3239		3735
3240	if (expect_true ((diff < 0. ? -diff : diff) < MIN_TIMEJUMP))	3736	if (ecb_expect_true ((diff < EV_TS_CONST (0.) ? -diff : diff) < EV_TS_CONST (MIN_TIMEJUMP)))
3241	return; /* all is well */	3737	return; /* all is well */
3242		3738
3243	ev_rt_now = ev_time ();	3739	ev_rt_now = ev_time ();
3244	mn_now = get_clock ();	3740	mn_now = get_clock ();
3245	now_floor = mn_now;	3741	now_floor = mn_now;
…		…
3254	else	3750	else
3255	#endif	3751	#endif
3256	{	3752	{
3257	ev_rt_now = ev_time ();	3753	ev_rt_now = ev_time ();
3258		3754
3259	if (expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + MIN_TIMEJUMP))	3755	if (ecb_expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + EV_TS_CONST (MIN_TIMEJUMP)))
3260	{	3756	{
3261	/* adjust timers. this is easy, as the offset is the same for all of them */	3757	/* adjust timers. this is easy, as the offset is the same for all of them */
3262	timers_reschedule (EV_A_ ev_rt_now - mn_now);	3758	timers_reschedule (EV_A_ ev_rt_now - mn_now);
3263	#if EV_PERIODIC_ENABLE	3759	#if EV_PERIODIC_ENABLE
3264	periodics_reschedule (EV_A);	3760	periodics_reschedule (EV_A);
…		…
3287	#if EV_VERIFY >= 2	3783	#if EV_VERIFY >= 2
3288	ev_verify (EV_A);	3784	ev_verify (EV_A);
3289	#endif	3785	#endif
3290		3786
3291	#ifndef _WIN32	3787	#ifndef _WIN32
3292	if (expect_false (curpid)) /* penalise the forking check even more */	3788	if (ecb_expect_false (curpid)) /* penalise the forking check even more */
3293	if (expect_false (getpid () != curpid))	3789	if (ecb_expect_false (getpid () != curpid))
3294	{	3790	{
3295	curpid = getpid ();	3791	curpid = getpid ();
3296	postfork = 1;	3792	postfork = 1;
3297	}	3793	}
3298	#endif	3794	#endif
3299		3795
3300	#if EV_FORK_ENABLE	3796	#if EV_FORK_ENABLE
3301	/* we might have forked, so queue fork handlers */	3797	/* we might have forked, so queue fork handlers */
3302	if (expect_false (postfork))	3798	if (ecb_expect_false (postfork))
3303	if (forkcnt)	3799	if (forkcnt)
3304	{	3800	{
3305	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);	3801	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);
3306	EV_INVOKE_PENDING;	3802	EV_INVOKE_PENDING;
3307	}	3803	}
3308	#endif	3804	#endif
3309		3805
3310	#if EV_PREPARE_ENABLE	3806	#if EV_PREPARE_ENABLE
3311	/* queue prepare watchers (and execute them) */	3807	/* queue prepare watchers (and execute them) */
3312	if (expect_false (preparecnt))	3808	if (ecb_expect_false (preparecnt))
3313	{	3809	{
3314	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);	3810	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);
3315	EV_INVOKE_PENDING;	3811	EV_INVOKE_PENDING;
3316	}	3812	}
3317	#endif	3813	#endif
3318		3814
3319	if (expect_false (loop_done))	3815	if (ecb_expect_false (loop_done))
3320	break;	3816	break;
3321		3817
3322	/* we might have forked, so reify kernel state if necessary */	3818	/* we might have forked, so reify kernel state if necessary */
3323	if (expect_false (postfork))	3819	if (ecb_expect_false (postfork))
3324	loop_fork (EV_A);	3820	loop_fork (EV_A);
3325		3821
3326	/* update fd-related kernel structures */	3822	/* update fd-related kernel structures */
3327	fd_reify (EV_A);	3823	fd_reify (EV_A);
3328		3824
…		…
3333		3829
3334	/* remember old timestamp for io_blocktime calculation */	3830	/* remember old timestamp for io_blocktime calculation */
3335	ev_tstamp prev_mn_now = mn_now;	3831	ev_tstamp prev_mn_now = mn_now;
3336		3832
3337	/* update time to cancel out callback processing overhead */	3833	/* update time to cancel out callback processing overhead */
3338	time_update (EV_A_ 1e100);	3834	time_update (EV_A_ EV_TS_CONST (EV_TSTAMP_HUGE));
3339		3835
3340	/* from now on, we want a pipe-wake-up */	3836	/* from now on, we want a pipe-wake-up */
3341	pipe_write_wanted = 1;	3837	pipe_write_wanted = 1;
3342		3838
3343	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */	3839	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */
3344		3840
3345	if (expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))	3841	if (ecb_expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))
3346	{	3842	{
3347	waittime = MAX_BLOCKTIME;	3843	waittime = EV_TS_CONST (MAX_BLOCKTIME);
3348		3844
3349	if (timercnt)	3845	if (timercnt)
3350	{	3846	{
3351	ev_tstamp to = ANHE_at (timers [HEAP0]) - mn_now;	3847	ev_tstamp to = ANHE_at (timers [HEAP0]) - mn_now;
3352	if (waittime > to) waittime = to;	3848	if (waittime > to) waittime = to;
…		…
3359	if (waittime > to) waittime = to;	3855	if (waittime > to) waittime = to;
3360	}	3856	}
3361	#endif	3857	#endif
3362		3858
3363	/* don't let timeouts decrease the waittime below timeout_blocktime */	3859	/* don't let timeouts decrease the waittime below timeout_blocktime */
3364	if (expect_false (waittime < timeout_blocktime))	3860	if (ecb_expect_false (waittime < timeout_blocktime))
3365	waittime = timeout_blocktime;	3861	waittime = timeout_blocktime;
3366		3862
3367	/* at this point, we NEED to wait, so we have to ensure */	3863	/* now there are two more special cases left, either we have
3368	/* to pass a minimum nonzero value to the backend */	3864	* already-expired timers, so we should not sleep, or we have timers
		3865	* that expire very soon, in which case we need to wait for a minimum
		3866	* amount of time for some event loop backends.
		3867	*/
3369	if (expect_false (waittime < backend_mintime))	3868	if (ecb_expect_false (waittime < backend_mintime))
		3869	waittime = waittime <= EV_TS_CONST (0.)
		3870	? EV_TS_CONST (0.)
3370	waittime = backend_mintime;	3871	: backend_mintime;
3371		3872
3372	/* extra check because io_blocktime is commonly 0 */	3873	/* extra check because io_blocktime is commonly 0 */
3373	if (expect_false (io_blocktime))	3874	if (ecb_expect_false (io_blocktime))
3374	{	3875	{
3375	sleeptime = io_blocktime - (mn_now - prev_mn_now);	3876	sleeptime = io_blocktime - (mn_now - prev_mn_now);
3376		3877
3377	if (sleeptime > waittime - backend_mintime)	3878	if (sleeptime > waittime - backend_mintime)
3378	sleeptime = waittime - backend_mintime;	3879	sleeptime = waittime - backend_mintime;
3379		3880
3380	if (expect_true (sleeptime > 0.))	3881	if (ecb_expect_true (sleeptime > EV_TS_CONST (0.)))
3381	{	3882	{
3382	ev_sleep (sleeptime);	3883	ev_sleep (sleeptime);
3383	waittime -= sleeptime;	3884	waittime -= sleeptime;
3384	}	3885	}
3385	}	3886	}
…		…
3399	{	3900	{
3400	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));	3901	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));
3401	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);	3902	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);
3402	}	3903	}
3403		3904
3404
3405	/* update ev_rt_now, do magic */	3905	/* update ev_rt_now, do magic */
3406	time_update (EV_A_ waittime + sleeptime);	3906	time_update (EV_A_ waittime + sleeptime);
3407	}	3907	}
3408		3908
3409	/* queue pending timers and reschedule them */	3909	/* queue pending timers and reschedule them */
…		…
3417	idle_reify (EV_A);	3917	idle_reify (EV_A);
3418	#endif	3918	#endif
3419		3919
3420	#if EV_CHECK_ENABLE	3920	#if EV_CHECK_ENABLE
3421	/* queue check watchers, to be executed first */	3921	/* queue check watchers, to be executed first */
3422	if (expect_false (checkcnt))	3922	if (ecb_expect_false (checkcnt))
3423	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);	3923	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);
3424	#endif	3924	#endif
3425		3925
3426	EV_INVOKE_PENDING;	3926	EV_INVOKE_PENDING;
3427	}	3927	}
3428	while (expect_true (	3928	while (ecb_expect_true (
3429	activecnt	3929	activecnt
3430	&& !loop_done	3930	&& !loop_done
3431	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))	3931	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))
3432	));	3932	));
3433		3933
…		…
3440		3940
3441	return activecnt;	3941	return activecnt;
3442	}	3942	}
3443		3943
3444	void	3944	void
3445	ev_break (EV_P_ int how) EV_THROW	3945	ev_break (EV_P_ int how) EV_NOEXCEPT
3446	{	3946	{
3447	loop_done = how;	3947	loop_done = how;
3448	}	3948	}
3449		3949
3450	void	3950	void
3451	ev_ref (EV_P) EV_THROW	3951	ev_ref (EV_P) EV_NOEXCEPT
3452	{	3952	{
3453	++activecnt;	3953	++activecnt;
3454	}	3954	}
3455		3955
3456	void	3956	void
3457	ev_unref (EV_P) EV_THROW	3957	ev_unref (EV_P) EV_NOEXCEPT
3458	{	3958	{
3459	--activecnt;	3959	--activecnt;
3460	}	3960	}
3461		3961
3462	void	3962	void
3463	ev_now_update (EV_P) EV_THROW	3963	ev_now_update (EV_P) EV_NOEXCEPT
3464	{	3964	{
3465	time_update (EV_A_ 1e100);	3965	time_update (EV_A_ EV_TSTAMP_HUGE);
3466	}	3966	}
3467		3967
3468	void	3968	void
3469	ev_suspend (EV_P) EV_THROW	3969	ev_suspend (EV_P) EV_NOEXCEPT
3470	{	3970	{
3471	ev_now_update (EV_A);	3971	ev_now_update (EV_A);
3472	}	3972	}
3473		3973
3474	void	3974	void
3475	ev_resume (EV_P) EV_THROW	3975	ev_resume (EV_P) EV_NOEXCEPT
3476	{	3976	{
3477	ev_tstamp mn_prev = mn_now;	3977	ev_tstamp mn_prev = mn_now;
3478		3978
3479	ev_now_update (EV_A);	3979	ev_now_update (EV_A);
3480	timers_reschedule (EV_A_ mn_now - mn_prev);	3980	timers_reschedule (EV_A_ mn_now - mn_prev);
…		…
3497	inline_size void	3997	inline_size void
3498	wlist_del (WL *head, WL elem)	3998	wlist_del (WL *head, WL elem)
3499	{	3999	{
3500	while (*head)	4000	while (*head)
3501	{	4001	{
3502	if (expect_true (*head == elem))	4002	if (ecb_expect_true (*head == elem))
3503	{	4003	{
3504	*head = elem->next;	4004	*head = elem->next;
3505	break;	4005	break;
3506	}	4006	}
3507		4007
…		…
3519	w->pending = 0;	4019	w->pending = 0;
3520	}	4020	}
3521	}	4021	}
3522		4022
3523	int	4023	int
3524	ev_clear_pending (EV_P_ void *w) EV_THROW	4024	ev_clear_pending (EV_P_ void *w) EV_NOEXCEPT
3525	{	4025	{
3526	W w_ = (W)w;	4026	W w_ = (W)w;
3527	int pending = w_->pending;	4027	int pending = w_->pending;
3528		4028
3529	if (expect_true (pending))	4029	if (ecb_expect_true (pending))
3530	{	4030	{
3531	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;	4031	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;
3532	p->w = (W)&pending_w;	4032	p->w = (W)&pending_w;
3533	w_->pending = 0;	4033	w_->pending = 0;
3534	return p->events;	4034	return p->events;
…		…
3561	w->active = 0;	4061	w->active = 0;
3562	}	4062	}
3563		4063
3564	/*****************************************************************************/	4064	/*****************************************************************************/
3565		4065
3566	void noinline	4066	ecb_noinline
		4067	void
3567	ev_io_start (EV_P_ ev_io *w) EV_THROW	4068	ev_io_start (EV_P_ ev_io *w) EV_NOEXCEPT
3568	{	4069	{
3569	int fd = w->fd;	4070	int fd = w->fd;
3570		4071
3571	if (expect_false (ev_is_active (w)))	4072	if (ecb_expect_false (ev_is_active (w)))
3572	return;	4073	return;
3573		4074
3574	assert (("libev: ev_io_start called with negative fd", fd >= 0));	4075	assert (("libev: ev_io_start called with negative fd", fd >= 0));
3575	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));	4076	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));
3576		4077
		4078	#if EV_VERIFY >= 2
		4079	assert (("libev: ev_io_start called on watcher with invalid fd", fd_valid (fd)));
		4080	#endif
3577	EV_FREQUENT_CHECK;	4081	EV_FREQUENT_CHECK;
3578		4082
3579	ev_start (EV_A_ (W)w, 1);	4083	ev_start (EV_A_ (W)w, 1);
3580	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_init_zero);	4084	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_needsize_zerofill);
3581	wlist_add (&anfds[fd].head, (WL)w);	4085	wlist_add (&anfds[fd].head, (WL)w);
3582		4086
3583	/* common bug, apparently */	4087	/* common bug, apparently */
3584	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));	4088	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));
3585		4089
…		…
3587	w->events &= ~EV__IOFDSET;	4091	w->events &= ~EV__IOFDSET;
3588		4092
3589	EV_FREQUENT_CHECK;	4093	EV_FREQUENT_CHECK;
3590	}	4094	}
3591		4095
3592	void noinline	4096	ecb_noinline
		4097	void
3593	ev_io_stop (EV_P_ ev_io *w) EV_THROW	4098	ev_io_stop (EV_P_ ev_io *w) EV_NOEXCEPT
3594	{	4099	{
3595	clear_pending (EV_A_ (W)w);	4100	clear_pending (EV_A_ (W)w);
3596	if (expect_false (!ev_is_active (w)))	4101	if (ecb_expect_false (!ev_is_active (w)))
3597	return;	4102	return;
3598		4103
3599	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));	4104	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));
3600		4105
		4106	#if EV_VERIFY >= 2
		4107	assert (("libev: ev_io_stop called on watcher with invalid fd", fd_valid (w->fd)));
		4108	#endif
3601	EV_FREQUENT_CHECK;	4109	EV_FREQUENT_CHECK;
3602		4110
3603	wlist_del (&anfds[w->fd].head, (WL)w);	4111	wlist_del (&anfds[w->fd].head, (WL)w);
3604	ev_stop (EV_A_ (W)w);	4112	ev_stop (EV_A_ (W)w);
3605		4113
3606	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);	4114	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);
3607		4115
3608	EV_FREQUENT_CHECK;	4116	EV_FREQUENT_CHECK;
3609	}	4117	}
3610		4118
3611	void noinline	4119	ecb_noinline
		4120	void
3612	ev_timer_start (EV_P_ ev_timer *w) EV_THROW	4121	ev_timer_start (EV_P_ ev_timer *w) EV_NOEXCEPT
3613	{	4122	{
3614	if (expect_false (ev_is_active (w)))	4123	if (ecb_expect_false (ev_is_active (w)))
3615	return;	4124	return;
3616		4125
3617	ev_at (w) += mn_now;	4126	ev_at (w) += mn_now;
3618		4127
3619	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));	4128	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));
3620		4129
3621	EV_FREQUENT_CHECK;	4130	EV_FREQUENT_CHECK;
3622		4131
3623	++timercnt;	4132	++timercnt;
3624	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);	4133	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);
3625	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, EMPTY2);	4134	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, array_needsize_noinit);
3626	ANHE_w (timers [ev_active (w)]) = (WT)w;	4135	ANHE_w (timers [ev_active (w)]) = (WT)w;
3627	ANHE_at_cache (timers [ev_active (w)]);	4136	ANHE_at_cache (timers [ev_active (w)]);
3628	upheap (timers, ev_active (w));	4137	upheap (timers, ev_active (w));
3629		4138
3630	EV_FREQUENT_CHECK;	4139	EV_FREQUENT_CHECK;
3631		4140
3632	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/	4141	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/
3633	}	4142	}
3634		4143
3635	void noinline	4144	ecb_noinline
		4145	void
3636	ev_timer_stop (EV_P_ ev_timer *w) EV_THROW	4146	ev_timer_stop (EV_P_ ev_timer *w) EV_NOEXCEPT
3637	{	4147	{
3638	clear_pending (EV_A_ (W)w);	4148	clear_pending (EV_A_ (W)w);
3639	if (expect_false (!ev_is_active (w)))	4149	if (ecb_expect_false (!ev_is_active (w)))
3640	return;	4150	return;
3641		4151
3642	EV_FREQUENT_CHECK;	4152	EV_FREQUENT_CHECK;
3643		4153
3644	{	4154	{
…		…
3646		4156
3647	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));	4157	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));
3648		4158
3649	--timercnt;	4159	--timercnt;
3650		4160
3651	if (expect_true (active < timercnt + HEAP0))	4161	if (ecb_expect_true (active < timercnt + HEAP0))
3652	{	4162	{
3653	timers [active] = timers [timercnt + HEAP0];	4163	timers [active] = timers [timercnt + HEAP0];
3654	adjustheap (timers, timercnt, active);	4164	adjustheap (timers, timercnt, active);
3655	}	4165	}
3656	}	4166	}
…		…
3660	ev_stop (EV_A_ (W)w);	4170	ev_stop (EV_A_ (W)w);
3661		4171
3662	EV_FREQUENT_CHECK;	4172	EV_FREQUENT_CHECK;
3663	}	4173	}
3664		4174
3665	void noinline	4175	ecb_noinline
		4176	void
3666	ev_timer_again (EV_P_ ev_timer *w) EV_THROW	4177	ev_timer_again (EV_P_ ev_timer *w) EV_NOEXCEPT
3667	{	4178	{
3668	EV_FREQUENT_CHECK;	4179	EV_FREQUENT_CHECK;
3669		4180
3670	clear_pending (EV_A_ (W)w);	4181	clear_pending (EV_A_ (W)w);
3671		4182
…		…
3688		4199
3689	EV_FREQUENT_CHECK;	4200	EV_FREQUENT_CHECK;
3690	}	4201	}
3691		4202
3692	ev_tstamp	4203	ev_tstamp
3693	ev_timer_remaining (EV_P_ ev_timer *w) EV_THROW	4204	ev_timer_remaining (EV_P_ ev_timer *w) EV_NOEXCEPT
3694	{	4205	{
3695	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);	4206	return ev_at (w) - (ev_is_active (w) ? mn_now : EV_TS_CONST (0.));
3696	}	4207	}
3697		4208
3698	#if EV_PERIODIC_ENABLE	4209	#if EV_PERIODIC_ENABLE
3699	void noinline	4210	ecb_noinline
		4211	void
3700	ev_periodic_start (EV_P_ ev_periodic *w) EV_THROW	4212	ev_periodic_start (EV_P_ ev_periodic *w) EV_NOEXCEPT
3701	{	4213	{
3702	if (expect_false (ev_is_active (w)))	4214	if (ecb_expect_false (ev_is_active (w)))
3703	return;	4215	return;
3704		4216
3705	if (w->reschedule_cb)	4217	if (w->reschedule_cb)
3706	ev_at (w) = w->reschedule_cb (w, ev_rt_now);	4218	ev_at (w) = w->reschedule_cb (w, ev_rt_now);
3707	else if (w->interval)	4219	else if (w->interval)
…		…
3714		4226
3715	EV_FREQUENT_CHECK;	4227	EV_FREQUENT_CHECK;
3716		4228
3717	++periodiccnt;	4229	++periodiccnt;
3718	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);	4230	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);
3719	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, EMPTY2);	4231	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, array_needsize_noinit);
3720	ANHE_w (periodics [ev_active (w)]) = (WT)w;	4232	ANHE_w (periodics [ev_active (w)]) = (WT)w;
3721	ANHE_at_cache (periodics [ev_active (w)]);	4233	ANHE_at_cache (periodics [ev_active (w)]);
3722	upheap (periodics, ev_active (w));	4234	upheap (periodics, ev_active (w));
3723		4235
3724	EV_FREQUENT_CHECK;	4236	EV_FREQUENT_CHECK;
3725		4237
3726	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/	4238	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/
3727	}	4239	}
3728		4240
3729	void noinline	4241	ecb_noinline
		4242	void
3730	ev_periodic_stop (EV_P_ ev_periodic *w) EV_THROW	4243	ev_periodic_stop (EV_P_ ev_periodic *w) EV_NOEXCEPT
3731	{	4244	{
3732	clear_pending (EV_A_ (W)w);	4245	clear_pending (EV_A_ (W)w);
3733	if (expect_false (!ev_is_active (w)))	4246	if (ecb_expect_false (!ev_is_active (w)))
3734	return;	4247	return;
3735		4248
3736	EV_FREQUENT_CHECK;	4249	EV_FREQUENT_CHECK;
3737		4250
3738	{	4251	{
…		…
3740		4253
3741	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));	4254	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));
3742		4255
3743	--periodiccnt;	4256	--periodiccnt;
3744		4257
3745	if (expect_true (active < periodiccnt + HEAP0))	4258	if (ecb_expect_true (active < periodiccnt + HEAP0))
3746	{	4259	{
3747	periodics [active] = periodics [periodiccnt + HEAP0];	4260	periodics [active] = periodics [periodiccnt + HEAP0];
3748	adjustheap (periodics, periodiccnt, active);	4261	adjustheap (periodics, periodiccnt, active);
3749	}	4262	}
3750	}	4263	}
…		…
3752	ev_stop (EV_A_ (W)w);	4265	ev_stop (EV_A_ (W)w);
3753		4266
3754	EV_FREQUENT_CHECK;	4267	EV_FREQUENT_CHECK;
3755	}	4268	}
3756		4269
3757	void noinline	4270	ecb_noinline
		4271	void
3758	ev_periodic_again (EV_P_ ev_periodic *w) EV_THROW	4272	ev_periodic_again (EV_P_ ev_periodic *w) EV_NOEXCEPT
3759	{	4273	{
3760	/* TODO: use adjustheap and recalculation */	4274	/* TODO: use adjustheap and recalculation */
3761	ev_periodic_stop (EV_A_ w);	4275	ev_periodic_stop (EV_A_ w);
3762	ev_periodic_start (EV_A_ w);	4276	ev_periodic_start (EV_A_ w);
3763	}	4277	}
…		…
3767	# define SA_RESTART 0	4281	# define SA_RESTART 0
3768	#endif	4282	#endif
3769		4283
3770	#if EV_SIGNAL_ENABLE	4284	#if EV_SIGNAL_ENABLE
3771		4285
3772	void noinline	4286	ecb_noinline
		4287	void
3773	ev_signal_start (EV_P_ ev_signal *w) EV_THROW	4288	ev_signal_start (EV_P_ ev_signal *w) EV_NOEXCEPT
3774	{	4289	{
3775	if (expect_false (ev_is_active (w)))	4290	if (ecb_expect_false (ev_is_active (w)))
3776	return;	4291	return;
3777		4292
3778	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));	4293	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));
3779		4294
3780	#if EV_MULTIPLICITY	4295	#if EV_MULTIPLICITY
…		…
3849	}	4364	}
3850		4365
3851	EV_FREQUENT_CHECK;	4366	EV_FREQUENT_CHECK;
3852	}	4367	}
3853		4368
3854	void noinline	4369	ecb_noinline
		4370	void
3855	ev_signal_stop (EV_P_ ev_signal *w) EV_THROW	4371	ev_signal_stop (EV_P_ ev_signal *w) EV_NOEXCEPT
3856	{	4372	{
3857	clear_pending (EV_A_ (W)w);	4373	clear_pending (EV_A_ (W)w);
3858	if (expect_false (!ev_is_active (w)))	4374	if (ecb_expect_false (!ev_is_active (w)))
3859	return;	4375	return;
3860		4376
3861	EV_FREQUENT_CHECK;	4377	EV_FREQUENT_CHECK;
3862		4378
3863	wlist_del (&signals [w->signum - 1].head, (WL)w);	4379	wlist_del (&signals [w->signum - 1].head, (WL)w);
…		…
3891	#endif	4407	#endif
3892		4408
3893	#if EV_CHILD_ENABLE	4409	#if EV_CHILD_ENABLE
3894		4410
3895	void	4411	void
3896	ev_child_start (EV_P_ ev_child *w) EV_THROW	4412	ev_child_start (EV_P_ ev_child *w) EV_NOEXCEPT
3897	{	4413	{
3898	#if EV_MULTIPLICITY	4414	#if EV_MULTIPLICITY
3899	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));	4415	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));
3900	#endif	4416	#endif
3901	if (expect_false (ev_is_active (w)))	4417	if (ecb_expect_false (ev_is_active (w)))
3902	return;	4418	return;
3903		4419
3904	EV_FREQUENT_CHECK;	4420	EV_FREQUENT_CHECK;
3905		4421
3906	ev_start (EV_A_ (W)w, 1);	4422	ev_start (EV_A_ (W)w, 1);
…		…
3908		4424
3909	EV_FREQUENT_CHECK;	4425	EV_FREQUENT_CHECK;
3910	}	4426	}
3911		4427
3912	void	4428	void
3913	ev_child_stop (EV_P_ ev_child *w) EV_THROW	4429	ev_child_stop (EV_P_ ev_child *w) EV_NOEXCEPT
3914	{	4430	{
3915	clear_pending (EV_A_ (W)w);	4431	clear_pending (EV_A_ (W)w);
3916	if (expect_false (!ev_is_active (w)))	4432	if (ecb_expect_false (!ev_is_active (w)))
3917	return;	4433	return;
3918		4434
3919	EV_FREQUENT_CHECK;	4435	EV_FREQUENT_CHECK;
3920		4436
3921	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);	4437	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);
…		…
3935		4451
3936	#define DEF_STAT_INTERVAL 5.0074891	4452	#define DEF_STAT_INTERVAL 5.0074891
3937	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */	4453	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */
3938	#define MIN_STAT_INTERVAL 0.1074891	4454	#define MIN_STAT_INTERVAL 0.1074891
3939		4455
3940	static void noinline stat_timer_cb (EV_P_ ev_timer *w_, int revents);	4456	ecb_noinline static void stat_timer_cb (EV_P_ ev_timer *w_, int revents);
3941		4457
3942	#if EV_USE_INOTIFY	4458	#if EV_USE_INOTIFY
3943		4459
3944	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */	4460	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */
3945	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)	4461	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)
3946		4462
3947	static void noinline	4463	ecb_noinline
		4464	static void
3948	infy_add (EV_P_ ev_stat *w)	4465	infy_add (EV_P_ ev_stat *w)
3949	{	4466	{
3950	w->wd = inotify_add_watch (fs_fd, w->path,	4467	w->wd = inotify_add_watch (fs_fd, w->path,
3951	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY	4468	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY
3952	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO	4469	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO
…		…
4016	if (ev_is_active (&w->timer)) ev_ref (EV_A);	4533	if (ev_is_active (&w->timer)) ev_ref (EV_A);
4017	ev_timer_again (EV_A_ &w->timer);	4534	ev_timer_again (EV_A_ &w->timer);
4018	if (ev_is_active (&w->timer)) ev_unref (EV_A);	4535	if (ev_is_active (&w->timer)) ev_unref (EV_A);
4019	}	4536	}
4020		4537
4021	static void noinline	4538	ecb_noinline
		4539	static void
4022	infy_del (EV_P_ ev_stat *w)	4540	infy_del (EV_P_ ev_stat *w)
4023	{	4541	{
4024	int slot;	4542	int slot;
4025	int wd = w->wd;	4543	int wd = w->wd;
4026		4544
…		…
4033		4551
4034	/* remove this watcher, if others are watching it, they will rearm */	4552	/* remove this watcher, if others are watching it, they will rearm */
4035	inotify_rm_watch (fs_fd, wd);	4553	inotify_rm_watch (fs_fd, wd);
4036	}	4554	}
4037		4555
4038	static void noinline	4556	ecb_noinline
		4557	static void
4039	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)	4558	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)
4040	{	4559	{
4041	if (slot < 0)	4560	if (slot < 0)
4042	/* overflow, need to check for all hash slots */	4561	/* overflow, need to check for all hash slots */
4043	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)	4562	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)
…		…
4079	infy_wd (EV_A_ ev->wd, ev->wd, ev);	4598	infy_wd (EV_A_ ev->wd, ev->wd, ev);
4080	ofs += sizeof (struct inotify_event) + ev->len;	4599	ofs += sizeof (struct inotify_event) + ev->len;
4081	}	4600	}
4082	}	4601	}
4083		4602
4084	inline_size void ecb_cold	4603	inline_size ecb_cold
		4604	void
4085	ev_check_2625 (EV_P)	4605	ev_check_2625 (EV_P)
4086	{	4606	{
4087	/* kernels < 2.6.25 are borked	4607	/* kernels < 2.6.25 are borked
4088	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html	4608	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html
4089	*/	4609	*/
…		…
4179	#else	4699	#else
4180	# define EV_LSTAT(p,b) lstat (p, b)	4700	# define EV_LSTAT(p,b) lstat (p, b)
4181	#endif	4701	#endif
4182		4702
4183	void	4703	void
4184	ev_stat_stat (EV_P_ ev_stat *w) EV_THROW	4704	ev_stat_stat (EV_P_ ev_stat *w) EV_NOEXCEPT
4185	{	4705	{
4186	if (lstat (w->path, &w->attr) < 0)	4706	if (lstat (w->path, &w->attr) < 0)
4187	w->attr.st_nlink = 0;	4707	w->attr.st_nlink = 0;
4188	else if (!w->attr.st_nlink)	4708	else if (!w->attr.st_nlink)
4189	w->attr.st_nlink = 1;	4709	w->attr.st_nlink = 1;
4190	}	4710	}
4191		4711
4192	static void noinline	4712	ecb_noinline
		4713	static void
4193	stat_timer_cb (EV_P_ ev_timer *w_, int revents)	4714	stat_timer_cb (EV_P_ ev_timer *w_, int revents)
4194	{	4715	{
4195	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));	4716	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));
4196		4717
4197	ev_statdata prev = w->attr;	4718	ev_statdata prev = w->attr;
…		…
4228	ev_feed_event (EV_A_ w, EV_STAT);	4749	ev_feed_event (EV_A_ w, EV_STAT);
4229	}	4750	}
4230	}	4751	}
4231		4752
4232	void	4753	void
4233	ev_stat_start (EV_P_ ev_stat *w) EV_THROW	4754	ev_stat_start (EV_P_ ev_stat *w) EV_NOEXCEPT
4234	{	4755	{
4235	if (expect_false (ev_is_active (w)))	4756	if (ecb_expect_false (ev_is_active (w)))
4236	return;	4757	return;
4237		4758
4238	ev_stat_stat (EV_A_ w);	4759	ev_stat_stat (EV_A_ w);
4239		4760
4240	if (w->interval < MIN_STAT_INTERVAL && w->interval)	4761	if (w->interval < MIN_STAT_INTERVAL && w->interval)
…		…
4259		4780
4260	EV_FREQUENT_CHECK;	4781	EV_FREQUENT_CHECK;
4261	}	4782	}
4262		4783
4263	void	4784	void
4264	ev_stat_stop (EV_P_ ev_stat *w) EV_THROW	4785	ev_stat_stop (EV_P_ ev_stat *w) EV_NOEXCEPT
4265	{	4786	{
4266	clear_pending (EV_A_ (W)w);	4787	clear_pending (EV_A_ (W)w);
4267	if (expect_false (!ev_is_active (w)))	4788	if (ecb_expect_false (!ev_is_active (w)))
4268	return;	4789	return;
4269		4790
4270	EV_FREQUENT_CHECK;	4791	EV_FREQUENT_CHECK;
4271		4792
4272	#if EV_USE_INOTIFY	4793	#if EV_USE_INOTIFY
…		…
4285	}	4806	}
4286	#endif	4807	#endif
4287		4808
4288	#if EV_IDLE_ENABLE	4809	#if EV_IDLE_ENABLE
4289	void	4810	void
4290	ev_idle_start (EV_P_ ev_idle *w) EV_THROW	4811	ev_idle_start (EV_P_ ev_idle *w) EV_NOEXCEPT
4291	{	4812	{
4292	if (expect_false (ev_is_active (w)))	4813	if (ecb_expect_false (ev_is_active (w)))
4293	return;	4814	return;
4294		4815
4295	pri_adjust (EV_A_ (W)w);	4816	pri_adjust (EV_A_ (W)w);
4296		4817
4297	EV_FREQUENT_CHECK;	4818	EV_FREQUENT_CHECK;
…		…
4300	int active = ++idlecnt [ABSPRI (w)];	4821	int active = ++idlecnt [ABSPRI (w)];
4301		4822
4302	++idleall;	4823	++idleall;
4303	ev_start (EV_A_ (W)w, active);	4824	ev_start (EV_A_ (W)w, active);
4304		4825
4305	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, EMPTY2);	4826	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, array_needsize_noinit);
4306	idles [ABSPRI (w)][active - 1] = w;	4827	idles [ABSPRI (w)][active - 1] = w;
4307	}	4828	}
4308		4829
4309	EV_FREQUENT_CHECK;	4830	EV_FREQUENT_CHECK;
4310	}	4831	}
4311		4832
4312	void	4833	void
4313	ev_idle_stop (EV_P_ ev_idle *w) EV_THROW	4834	ev_idle_stop (EV_P_ ev_idle *w) EV_NOEXCEPT
4314	{	4835	{
4315	clear_pending (EV_A_ (W)w);	4836	clear_pending (EV_A_ (W)w);
4316	if (expect_false (!ev_is_active (w)))	4837	if (ecb_expect_false (!ev_is_active (w)))
4317	return;	4838	return;
4318		4839
4319	EV_FREQUENT_CHECK;	4840	EV_FREQUENT_CHECK;
4320		4841
4321	{	4842	{
…		…
4332	}	4853	}
4333	#endif	4854	#endif
4334		4855
4335	#if EV_PREPARE_ENABLE	4856	#if EV_PREPARE_ENABLE
4336	void	4857	void
4337	ev_prepare_start (EV_P_ ev_prepare *w) EV_THROW	4858	ev_prepare_start (EV_P_ ev_prepare *w) EV_NOEXCEPT
4338	{	4859	{
4339	if (expect_false (ev_is_active (w)))	4860	if (ecb_expect_false (ev_is_active (w)))
4340	return;	4861	return;
4341		4862
4342	EV_FREQUENT_CHECK;	4863	EV_FREQUENT_CHECK;
4343		4864
4344	ev_start (EV_A_ (W)w, ++preparecnt);	4865	ev_start (EV_A_ (W)w, ++preparecnt);
4345	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, EMPTY2);	4866	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, array_needsize_noinit);
4346	prepares [preparecnt - 1] = w;	4867	prepares [preparecnt - 1] = w;
4347		4868
4348	EV_FREQUENT_CHECK;	4869	EV_FREQUENT_CHECK;
4349	}	4870	}
4350		4871
4351	void	4872	void
4352	ev_prepare_stop (EV_P_ ev_prepare *w) EV_THROW	4873	ev_prepare_stop (EV_P_ ev_prepare *w) EV_NOEXCEPT
4353	{	4874	{
4354	clear_pending (EV_A_ (W)w);	4875	clear_pending (EV_A_ (W)w);
4355	if (expect_false (!ev_is_active (w)))	4876	if (ecb_expect_false (!ev_is_active (w)))
4356	return;	4877	return;
4357		4878
4358	EV_FREQUENT_CHECK;	4879	EV_FREQUENT_CHECK;
4359		4880
4360	{	4881	{
…		…
4370	}	4891	}
4371	#endif	4892	#endif
4372		4893
4373	#if EV_CHECK_ENABLE	4894	#if EV_CHECK_ENABLE
4374	void	4895	void
4375	ev_check_start (EV_P_ ev_check *w) EV_THROW	4896	ev_check_start (EV_P_ ev_check *w) EV_NOEXCEPT
4376	{	4897	{
4377	if (expect_false (ev_is_active (w)))	4898	if (ecb_expect_false (ev_is_active (w)))
4378	return;	4899	return;
4379		4900
4380	EV_FREQUENT_CHECK;	4901	EV_FREQUENT_CHECK;
4381		4902
4382	ev_start (EV_A_ (W)w, ++checkcnt);	4903	ev_start (EV_A_ (W)w, ++checkcnt);
4383	array_needsize (ev_check *, checks, checkmax, checkcnt, EMPTY2);	4904	array_needsize (ev_check *, checks, checkmax, checkcnt, array_needsize_noinit);
4384	checks [checkcnt - 1] = w;	4905	checks [checkcnt - 1] = w;
4385		4906
4386	EV_FREQUENT_CHECK;	4907	EV_FREQUENT_CHECK;
4387	}	4908	}
4388		4909
4389	void	4910	void
4390	ev_check_stop (EV_P_ ev_check *w) EV_THROW	4911	ev_check_stop (EV_P_ ev_check *w) EV_NOEXCEPT
4391	{	4912	{
4392	clear_pending (EV_A_ (W)w);	4913	clear_pending (EV_A_ (W)w);
4393	if (expect_false (!ev_is_active (w)))	4914	if (ecb_expect_false (!ev_is_active (w)))
4394	return;	4915	return;
4395		4916
4396	EV_FREQUENT_CHECK;	4917	EV_FREQUENT_CHECK;
4397		4918
4398	{	4919	{
…		…
4407	EV_FREQUENT_CHECK;	4928	EV_FREQUENT_CHECK;
4408	}	4929	}
4409	#endif	4930	#endif
4410		4931
4411	#if EV_EMBED_ENABLE	4932	#if EV_EMBED_ENABLE
4412	void noinline	4933	ecb_noinline
		4934	void
4413	ev_embed_sweep (EV_P_ ev_embed *w) EV_THROW	4935	ev_embed_sweep (EV_P_ ev_embed *w) EV_NOEXCEPT
4414	{	4936	{
4415	ev_run (w->other, EVRUN_NOWAIT);	4937	ev_run (w->other, EVRUN_NOWAIT);
4416	}	4938	}
4417		4939
4418	static void	4940	static void
…		…
4466	ev_idle_stop (EV_A_ idle);	4988	ev_idle_stop (EV_A_ idle);
4467	}	4989	}
4468	#endif	4990	#endif
4469		4991
4470	void	4992	void
4471	ev_embed_start (EV_P_ ev_embed *w) EV_THROW	4993	ev_embed_start (EV_P_ ev_embed *w) EV_NOEXCEPT
4472	{	4994	{
4473	if (expect_false (ev_is_active (w)))	4995	if (ecb_expect_false (ev_is_active (w)))
4474	return;	4996	return;
4475		4997
4476	{	4998	{
4477	EV_P = w->other;	4999	EV_P = w->other;
4478	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));	5000	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));
…		…
4497		5019
4498	EV_FREQUENT_CHECK;	5020	EV_FREQUENT_CHECK;
4499	}	5021	}
4500		5022
4501	void	5023	void
4502	ev_embed_stop (EV_P_ ev_embed *w) EV_THROW	5024	ev_embed_stop (EV_P_ ev_embed *w) EV_NOEXCEPT
4503	{	5025	{
4504	clear_pending (EV_A_ (W)w);	5026	clear_pending (EV_A_ (W)w);
4505	if (expect_false (!ev_is_active (w)))	5027	if (ecb_expect_false (!ev_is_active (w)))
4506	return;	5028	return;
4507		5029
4508	EV_FREQUENT_CHECK;	5030	EV_FREQUENT_CHECK;
4509		5031
4510	ev_io_stop (EV_A_ &w->io);	5032	ev_io_stop (EV_A_ &w->io);
…		…
4517	}	5039	}
4518	#endif	5040	#endif
4519		5041
4520	#if EV_FORK_ENABLE	5042	#if EV_FORK_ENABLE
4521	void	5043	void
4522	ev_fork_start (EV_P_ ev_fork *w) EV_THROW	5044	ev_fork_start (EV_P_ ev_fork *w) EV_NOEXCEPT
4523	{	5045	{
4524	if (expect_false (ev_is_active (w)))	5046	if (ecb_expect_false (ev_is_active (w)))
4525	return;	5047	return;
4526		5048
4527	EV_FREQUENT_CHECK;	5049	EV_FREQUENT_CHECK;
4528		5050
4529	ev_start (EV_A_ (W)w, ++forkcnt);	5051	ev_start (EV_A_ (W)w, ++forkcnt);
4530	array_needsize (ev_fork *, forks, forkmax, forkcnt, EMPTY2);	5052	array_needsize (ev_fork *, forks, forkmax, forkcnt, array_needsize_noinit);
4531	forks [forkcnt - 1] = w;	5053	forks [forkcnt - 1] = w;
4532		5054
4533	EV_FREQUENT_CHECK;	5055	EV_FREQUENT_CHECK;
4534	}	5056	}
4535		5057
4536	void	5058	void
4537	ev_fork_stop (EV_P_ ev_fork *w) EV_THROW	5059	ev_fork_stop (EV_P_ ev_fork *w) EV_NOEXCEPT
4538	{	5060	{
4539	clear_pending (EV_A_ (W)w);	5061	clear_pending (EV_A_ (W)w);
4540	if (expect_false (!ev_is_active (w)))	5062	if (ecb_expect_false (!ev_is_active (w)))
4541	return;	5063	return;
4542		5064
4543	EV_FREQUENT_CHECK;	5065	EV_FREQUENT_CHECK;
4544		5066
4545	{	5067	{
…		…
4555	}	5077	}
4556	#endif	5078	#endif
4557		5079
4558	#if EV_CLEANUP_ENABLE	5080	#if EV_CLEANUP_ENABLE
4559	void	5081	void
4560	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_THROW	5082	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4561	{	5083	{
4562	if (expect_false (ev_is_active (w)))	5084	if (ecb_expect_false (ev_is_active (w)))
4563	return;	5085	return;
4564		5086
4565	EV_FREQUENT_CHECK;	5087	EV_FREQUENT_CHECK;
4566		5088
4567	ev_start (EV_A_ (W)w, ++cleanupcnt);	5089	ev_start (EV_A_ (W)w, ++cleanupcnt);
4568	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, EMPTY2);	5090	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, array_needsize_noinit);
4569	cleanups [cleanupcnt - 1] = w;	5091	cleanups [cleanupcnt - 1] = w;
4570		5092
4571	/* cleanup watchers should never keep a refcount on the loop */	5093	/* cleanup watchers should never keep a refcount on the loop */
4572	ev_unref (EV_A);	5094	ev_unref (EV_A);
4573	EV_FREQUENT_CHECK;	5095	EV_FREQUENT_CHECK;
4574	}	5096	}
4575		5097
4576	void	5098	void
4577	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_THROW	5099	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4578	{	5100	{
4579	clear_pending (EV_A_ (W)w);	5101	clear_pending (EV_A_ (W)w);
4580	if (expect_false (!ev_is_active (w)))	5102	if (ecb_expect_false (!ev_is_active (w)))
4581	return;	5103	return;
4582		5104
4583	EV_FREQUENT_CHECK;	5105	EV_FREQUENT_CHECK;
4584	ev_ref (EV_A);	5106	ev_ref (EV_A);
4585		5107
…		…
4596	}	5118	}
4597	#endif	5119	#endif
4598		5120
4599	#if EV_ASYNC_ENABLE	5121	#if EV_ASYNC_ENABLE
4600	void	5122	void
4601	ev_async_start (EV_P_ ev_async *w) EV_THROW	5123	ev_async_start (EV_P_ ev_async *w) EV_NOEXCEPT
4602	{	5124	{
4603	if (expect_false (ev_is_active (w)))	5125	if (ecb_expect_false (ev_is_active (w)))
4604	return;	5126	return;
4605		5127
4606	w->sent = 0;	5128	w->sent = 0;
4607		5129
4608	evpipe_init (EV_A);	5130	evpipe_init (EV_A);
4609		5131
4610	EV_FREQUENT_CHECK;	5132	EV_FREQUENT_CHECK;
4611		5133
4612	ev_start (EV_A_ (W)w, ++asynccnt);	5134	ev_start (EV_A_ (W)w, ++asynccnt);
4613	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, EMPTY2);	5135	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, array_needsize_noinit);
4614	asyncs [asynccnt - 1] = w;	5136	asyncs [asynccnt - 1] = w;
4615		5137
4616	EV_FREQUENT_CHECK;	5138	EV_FREQUENT_CHECK;
4617	}	5139	}
4618		5140
4619	void	5141	void
4620	ev_async_stop (EV_P_ ev_async *w) EV_THROW	5142	ev_async_stop (EV_P_ ev_async *w) EV_NOEXCEPT
4621	{	5143	{
4622	clear_pending (EV_A_ (W)w);	5144	clear_pending (EV_A_ (W)w);
4623	if (expect_false (!ev_is_active (w)))	5145	if (ecb_expect_false (!ev_is_active (w)))
4624	return;	5146	return;
4625		5147
4626	EV_FREQUENT_CHECK;	5148	EV_FREQUENT_CHECK;
4627		5149
4628	{	5150	{
…		…
4636		5158
4637	EV_FREQUENT_CHECK;	5159	EV_FREQUENT_CHECK;
4638	}	5160	}
4639		5161
4640	void	5162	void
4641	ev_async_send (EV_P_ ev_async *w) EV_THROW	5163	ev_async_send (EV_P_ ev_async *w) EV_NOEXCEPT
4642	{	5164	{
4643	w->sent = 1;	5165	w->sent = 1;
4644	evpipe_write (EV_A_ &async_pending);	5166	evpipe_write (EV_A_ &async_pending);
4645	}	5167	}
4646	#endif	5168	#endif
…		…
4683		5205
4684	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));	5206	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));
4685	}	5207	}
4686		5208
4687	void	5209	void
4688	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_THROW	5210	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_NOEXCEPT
4689	{	5211	{
4690	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));	5212	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));
4691
4692	if (expect_false (!once))
4693	{
4694	cb (EV_ERROR | EV_READ | EV_WRITE | EV_TIMER, arg);
4695	return;
4696	}
4697		5213
4698	once->cb = cb;	5214	once->cb = cb;
4699	once->arg = arg;	5215	once->arg = arg;
4700		5216
4701	ev_init (&once->io, once_cb_io);	5217	ev_init (&once->io, once_cb_io);
…		…
4714	}	5230	}
4715		5231
4716	/*****************************************************************************/	5232	/*****************************************************************************/
4717		5233
4718	#if EV_WALK_ENABLE	5234	#if EV_WALK_ENABLE
4719	void ecb_cold	5235	ecb_cold
		5236	void
4720	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_THROW	5237	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_NOEXCEPT
4721	{	5238	{
4722	int i, j;	5239	int i, j;
4723	ev_watcher_list *wl, *wn;	5240	ev_watcher_list *wl, *wn;
4724		5241
4725	if (types & (EV_IO | EV_EMBED))	5242	if (types & (EV_IO | EV_EMBED))

Diff Legend

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