ViewVC Help

View File | Revision Log | Show Annotations | Download File

/cvs/libev/ev.c

Comparing libev/ev.c (file contents):
Revision 1.464 by root, Fri Mar 21 16:41:04 2014 UTC vs.
Revision 1.510 by root, Wed Aug 28 09:45:49 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,2013 Marc Alexander Lehmann <libev@schmorp.de>	4	* Copyright (c) 2007-2019 Marc Alexander Lehmann <libev@schmorp.de>
5	* All rights reserved.	5	* All rights reserved.
6	*	6	*
7	* Redistribution and use in source and binary forms, with or without modifica-	7	* Redistribution and use in source and binary forms, with or without modifica-
8	* tion, are permitted provided that the following conditions are met:	8	* tion, are permitted provided that the following conditions are met:
9	*	9	*
…		…
43	# include EV_CONFIG_H	43	# include EV_CONFIG_H
44	# else	44	# else
45	# include "config.h"	45	# include "config.h"
46	# endif	46	# endif
47		47
48	#if HAVE_FLOOR	48	# if HAVE_FLOOR
49	# ifndef EV_USE_FLOOR	49	# ifndef EV_USE_FLOOR
50	# define EV_USE_FLOOR 1	50	# define EV_USE_FLOOR 1
		51	# endif
51	# endif	52	# endif
52	#endif
53		53
54	# if HAVE_CLOCK_SYSCALL	54	# if HAVE_CLOCK_SYSCALL
55	# ifndef EV_USE_CLOCK_SYSCALL	55	# ifndef EV_USE_CLOCK_SYSCALL
56	# define EV_USE_CLOCK_SYSCALL 1	56	# define EV_USE_CLOCK_SYSCALL 1
57	# ifndef EV_USE_REALTIME	57	# ifndef EV_USE_REALTIME
…		…
113	# define EV_USE_EPOLL EV_FEATURE_BACKENDS	113	# define EV_USE_EPOLL EV_FEATURE_BACKENDS
114	# endif	114	# endif
115	# else	115	# else
116	# undef EV_USE_EPOLL	116	# undef EV_USE_EPOLL
117	# define EV_USE_EPOLL 0	117	# define EV_USE_EPOLL 0
		118	# endif
		119
		120	# if HAVE_LINUX_AIO_ABI_H
		121	# ifndef EV_USE_LINUXAIO
		122	# define EV_USE_LINUXAIO EV_FEATURE_BACKENDS
		123	# endif
		124	# else
		125	# undef EV_USE_LINUXAIO
		126	# define EV_USE_LINUXAIO 0
118	# endif	127	# endif
119		128
120	# if HAVE_KQUEUE && HAVE_SYS_EVENT_H	129	# if HAVE_KQUEUE && HAVE_SYS_EVENT_H
121	# ifndef EV_USE_KQUEUE	130	# ifndef EV_USE_KQUEUE
122	# define EV_USE_KQUEUE EV_FEATURE_BACKENDS	131	# define EV_USE_KQUEUE EV_FEATURE_BACKENDS
…		…
162	# define EV_USE_EVENTFD 0	171	# define EV_USE_EVENTFD 0
163	# endif	172	# endif
164		173
165	#endif	174	#endif
166		175
		176	/* OS X, in its infinite idiocy, actually HARDCODES
		177	* a limit of 1024 into their select. Where people have brains,
		178	* OS X engineers apparently have a vacuum. Or maybe they were
		179	* ordered to have a vacuum, or they do anything for money.
		180	* This might help. Or not.
		181	* Note that this must be defined early, as other include files
		182	* will rely on this define as well.
		183	*/
		184	#define _DARWIN_UNLIMITED_SELECT 1
		185
167	#include <stdlib.h>	186	#include <stdlib.h>
168	#include <string.h>	187	#include <string.h>
169	#include <fcntl.h>	188	#include <fcntl.h>
170	#include <stddef.h>	189	#include <stddef.h>
171		190
…		…
208	# ifndef EV_SELECT_IS_WINSOCKET	227	# ifndef EV_SELECT_IS_WINSOCKET
209	# define EV_SELECT_IS_WINSOCKET 1	228	# define EV_SELECT_IS_WINSOCKET 1
210	# endif	229	# endif
211	# undef EV_AVOID_STDIO	230	# undef EV_AVOID_STDIO
212	#endif	231	#endif
213
214	/* OS X, in its infinite idiocy, actually HARDCODES
215	* a limit of 1024 into their select. Where people have brains,
216	* OS X engineers apparently have a vacuum. Or maybe they were
217	* ordered to have a vacuum, or they do anything for money.
218	* This might help. Or not.
219	*/
220	#define _DARWIN_UNLIMITED_SELECT 1
221		232
222	/* this block tries to deduce configuration from header-defined symbols and defaults */	233	/* this block tries to deduce configuration from header-defined symbols and defaults */
223		234
224	/* try to deduce the maximum number of signals on this platform */	235	/* try to deduce the maximum number of signals on this platform */
225	#if defined EV_NSIG	236	#if defined EV_NSIG
…		…
256	# else	267	# else
257	# define EV_USE_CLOCK_SYSCALL 0	268	# define EV_USE_CLOCK_SYSCALL 0
258	# endif	269	# endif
259	#endif	270	#endif
260		271
		272	#if !(_POSIX_TIMERS > 0)
		273	# ifndef EV_USE_MONOTONIC
		274	# define EV_USE_MONOTONIC 0
		275	# endif
		276	# ifndef EV_USE_REALTIME
		277	# define EV_USE_REALTIME 0
		278	# endif
		279	#endif
		280
261	#ifndef EV_USE_MONOTONIC	281	#ifndef EV_USE_MONOTONIC
262	# if defined _POSIX_MONOTONIC_CLOCK && _POSIX_MONOTONIC_CLOCK >= 0	282	# if defined _POSIX_MONOTONIC_CLOCK && _POSIX_MONOTONIC_CLOCK >= 0
263	# define EV_USE_MONOTONIC EV_FEATURE_OS	283	# define EV_USE_MONOTONIC EV_FEATURE_OS
264	# else	284	# else
265	# define EV_USE_MONOTONIC 0	285	# define EV_USE_MONOTONIC 0
…		…
304		324
305	#ifndef EV_USE_PORT	325	#ifndef EV_USE_PORT
306	# define EV_USE_PORT 0	326	# define EV_USE_PORT 0
307	#endif	327	#endif
308		328
		329	#ifndef EV_USE_LINUXAIO
		330	# if __linux /* libev currently assumes linux/aio_abi.h is always available on linux */
		331	# define EV_USE_LINUXAIO 1
		332	# else
		333	# define EV_USE_LINUXAIO 0
		334	# endif
		335	#endif
		336
		337	#ifndef EV_USE_IOURING
		338	# if __linux
		339	# define EV_USE_IOURING 0
		340	# else
		341	# define EV_USE_IOURING 0
		342	# endif
		343	#endif
		344
309	#ifndef EV_USE_INOTIFY	345	#ifndef EV_USE_INOTIFY
310	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))	346	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))
311	# define EV_USE_INOTIFY EV_FEATURE_OS	347	# define EV_USE_INOTIFY EV_FEATURE_OS
312	# else	348	# else
313	# define EV_USE_INOTIFY 0	349	# define EV_USE_INOTIFY 0
…		…
354		390
355	#ifndef EV_HEAP_CACHE_AT	391	#ifndef EV_HEAP_CACHE_AT
356	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA	392	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA
357	#endif	393	#endif
358		394
359	#ifdef ANDROID	395	#ifdef __ANDROID__
360	/* supposedly, android doesn't typedef fd_mask */	396	/* supposedly, android doesn't typedef fd_mask */
361	# undef EV_USE_SELECT	397	# undef EV_USE_SELECT
362	# define EV_USE_SELECT 0	398	# define EV_USE_SELECT 0
363	/* supposedly, we need to include syscall.h, not sys/syscall.h, so just disable */	399	/* supposedly, we need to include syscall.h, not sys/syscall.h, so just disable */
364	# undef EV_USE_CLOCK_SYSCALL	400	# undef EV_USE_CLOCK_SYSCALL
…		…
378	# include <sys/syscall.h>	414	# include <sys/syscall.h>
379	# ifdef SYS_clock_gettime	415	# ifdef SYS_clock_gettime
380	# define clock_gettime(id, ts) syscall (SYS_clock_gettime, (id), (ts))	416	# define clock_gettime(id, ts) syscall (SYS_clock_gettime, (id), (ts))
381	# undef EV_USE_MONOTONIC	417	# undef EV_USE_MONOTONIC
382	# define EV_USE_MONOTONIC 1	418	# define EV_USE_MONOTONIC 1
		419	# define EV_NEED_SYSCALL 1
383	# else	420	# else
384	# undef EV_USE_CLOCK_SYSCALL	421	# undef EV_USE_CLOCK_SYSCALL
385	# define EV_USE_CLOCK_SYSCALL 0	422	# define EV_USE_CLOCK_SYSCALL 0
386	# endif	423	# endif
387	#endif	424	#endif
…		…
405		442
406	#if !EV_USE_NANOSLEEP	443	#if !EV_USE_NANOSLEEP
407	/* hp-ux has it in sys/time.h, which we unconditionally include above */	444	/* hp-ux has it in sys/time.h, which we unconditionally include above */
408	# if !defined _WIN32 && !defined __hpux	445	# if !defined _WIN32 && !defined __hpux
409	# include <sys/select.h>	446	# include <sys/select.h>
		447	# endif
		448	#endif
		449
		450	#if EV_USE_LINUXAIO
		451	# include <sys/syscall.h>
		452	# if SYS_io_getevents && EV_USE_EPOLL /* linuxaio backend requires epoll backend */
		453	# define EV_NEED_SYSCALL 1
		454	# else
		455	# undef EV_USE_LINUXAIO
		456	# define EV_USE_LINUXAIO 0
		457	# endif
		458	#endif
		459
		460	#if EV_USE_IOURING
		461	# include <sys/syscall.h>
		462	# if !SYS_io_uring_setup && __linux && !__alpha
		463	# define SYS_io_uring_setup 425
		464	# define SYS_io_uring_enter 426
		465	# define SYS_io_uring_wregister 427
		466	# endif
		467	# if SYS_io_uring_setup && EV_USE_EPOLL /* iouring backend requires epoll backend */
		468	# define EV_NEED_SYSCALL 1
		469	# else
		470	# undef EV_USE_IOURING
		471	# define EV_USE_IOURING 0
410	# endif	472	# endif
411	#endif	473	#endif
412		474
413	#if EV_USE_INOTIFY	475	#if EV_USE_INOTIFY
414	# include <sys/statfs.h>	476	# include <sys/statfs.h>
…		…
456	uint32_t ssi_signo;	518	uint32_t ssi_signo;
457	char pad[128 - sizeof (uint32_t)];	519	char pad[128 - sizeof (uint32_t)];
458	};	520	};
459	#endif	521	#endif
460		522
461	/**/	523	/*****************************************************************************/
462		524
463	#if EV_VERIFY >= 3	525	#if EV_VERIFY >= 3
464	# define EV_FREQUENT_CHECK ev_verify (EV_A)	526	# define EV_FREQUENT_CHECK ev_verify (EV_A)
465	#else	527	#else
466	# define EV_FREQUENT_CHECK do { } while (0)	528	# define EV_FREQUENT_CHECK do { } while (0)
…		…
471	* This value is good at least till the year 4000.	533	* This value is good at least till the year 4000.
472	*/	534	*/
473	#define MIN_INTERVAL 0.0001220703125 /* 1/2**13, good till 4000 */	535	#define MIN_INTERVAL 0.0001220703125 /* 1/2**13, good till 4000 */
474	/*#define MIN_INTERVAL 0.00000095367431640625 /* 1/2**20, good till 2200 */	536	/*#define MIN_INTERVAL 0.00000095367431640625 /* 1/2**20, good till 2200 */
475		537
476	#define MIN_TIMEJUMP 1. /* minimum timejump that gets detected (if monotonic clock available) */	538	#define MIN_TIMEJUMP 1. /* minimum timejump that gets detected (if monotonic clock available) */
477	#define MAX_BLOCKTIME 59.743 /* never wait longer than this time (to detect time jumps) */	539	#define MAX_BLOCKTIME 59.743 /* never wait longer than this time (to detect time jumps) */
478		540
		541	/* find a portable timestamp that is "always" in the future but fits into time_t.
		542	* this is quite hard, and we are mostly guessing - we handle 32 bit signed/unsigned time_t,
		543	* and sizes larger than 32 bit, and maybe the unlikely floating point time_t */
		544	#define EV_TSTAMP_HUGE \
		545	(sizeof (time_t) >= 8 ? 10000000000000. \
		546	: 0 < (time_t)4294967295 ? 4294967295. \
		547	: 2147483647.) \
		548
		549	#ifndef EV_TS_CONST
		550	# define EV_TS_CONST(nv) nv
		551	# define EV_TS_TO_MSEC(a) a * 1e3 + 0.9999
		552	# 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)	553	# 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)	554	# define EV_TS_SET(ts,t) do { ts.tv_sec = (long)t; ts.tv_nsec = (long)((t - ts.tv_sec) * 1e9); } while (0)
		555	# define EV_TV_GET(tv) ((tv).tv_sec + (tv).tv_usec * 1e-6)
		556	# define EV_TS_GET(ts) ((ts).tv_sec + (ts).tv_nsec * 1e-9)
		557	#endif
481		558
482	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */	559	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */
483	/* ECB.H BEGIN */	560	/* ECB.H BEGIN */
484	/*	561	/*
485	* libecb - http://software.schmorp.de/pkg/libecb	562	* libecb - http://software.schmorp.de/pkg/libecb
486	*	563	*
487	* Copyright (©) 2009-2014 Marc Alexander Lehmann <libecb@schmorp.de>	564	* Copyright (©) 2009-2015 Marc Alexander Lehmann <libecb@schmorp.de>
488	* Copyright (©) 2011 Emanuele Giaquinta	565	* Copyright (©) 2011 Emanuele Giaquinta
489	* All rights reserved.	566	* All rights reserved.
490	*	567	*
491	* Redistribution and use in source and binary forms, with or without modifica-	568	* Redistribution and use in source and binary forms, with or without modifica-
492	* tion, are permitted provided that the following conditions are met:	569	* tion, are permitted provided that the following conditions are met:
…		…
506	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;	583	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;
507	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,	584	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,
508	* WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING NEGLIGENCE OR OTH-	585	* 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	586	* ERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED
510	* OF THE POSSIBILITY OF SUCH DAMAGE.	587	* OF THE POSSIBILITY OF SUCH DAMAGE.
		588	*
		589	* Alternatively, the contents of this file may be used under the terms of
		590	* the GNU General Public License ("GPL") version 2 or any later version,
		591	* in which case the provisions of the GPL are applicable instead of
		592	* the above. If you wish to allow the use of your version of this file
		593	* only under the terms of the GPL and not to allow others to use your
		594	* version of this file under the BSD license, indicate your decision
		595	* by deleting the provisions above and replace them with the notice
		596	* and other provisions required by the GPL. If you do not delete the
		597	* provisions above, a recipient may use your version of this file under
		598	* either the BSD or the GPL.
511	*/	599	*/
512		600
513	#ifndef ECB_H	601	#ifndef ECB_H
514	#define ECB_H	602	#define ECB_H
515		603
516	/* 16 bits major, 16 bits minor */	604	/* 16 bits major, 16 bits minor */
517	#define ECB_VERSION 0x00010003	605	#define ECB_VERSION 0x00010006
518		606
519	#ifdef _WIN32	607	#ifdef _WIN32
520	typedef signed char int8_t;	608	typedef signed char int8_t;
521	typedef unsigned char uint8_t;	609	typedef unsigned char uint8_t;
522	typedef signed short int16_t;	610	typedef signed short int16_t;
…		…
539	typedef uint32_t uintptr_t;	627	typedef uint32_t uintptr_t;
540	typedef int32_t intptr_t;	628	typedef int32_t intptr_t;
541	#endif	629	#endif
542	#else	630	#else
543	#include <inttypes.h>	631	#include <inttypes.h>
544	#if UINTMAX_MAX > 0xffffffffU	632	#if (defined INTPTR_MAX ? INTPTR_MAX : ULONG_MAX) > 0xffffffffU
545	#define ECB_PTRSIZE 8	633	#define ECB_PTRSIZE 8
546	#else	634	#else
547	#define ECB_PTRSIZE 4	635	#define ECB_PTRSIZE 4
548	#endif	636	#endif
549	#endif	637	#endif
550		638
		639	#define ECB_GCC_AMD64 (__amd64 || __amd64__ || __x86_64 || __x86_64__)
		640	#define ECB_MSVC_AMD64 (_M_AMD64 || _M_X64)
		641
551	/* work around x32 idiocy by defining proper macros */	642	/* work around x32 idiocy by defining proper macros */
552	#if __amd64 || __x86_64 || _M_AMD64 || _M_X64	643	#if ECB_GCC_AMD64 || ECB_MSVC_AMD64
553	#if _ILP32	644	#if _ILP32
554	#define ECB_AMD64_X32 1	645	#define ECB_AMD64_X32 1
555	#else	646	#else
556	#define ECB_AMD64 1	647	#define ECB_AMD64 1
557	#endif	648	#endif
…		…
562	* causing enormous grief in return for some better fake benchmark numbers.	653	* causing enormous grief in return for some better fake benchmark numbers.
563	* or so.	654	* or so.
564	* we try to detect these and simply assume they are not gcc - if they have	655	* 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.	656	* an issue with that they should have done it right in the first place.
566	*/	657	*/
567	#ifndef ECB_GCC_VERSION
568	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__	658	#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	659	#define ECB_GCC_VERSION(major,minor) 0
570	#else	660	#else
571	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))	661	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))
572	#endif	662	#endif
		663
		664	#define ECB_CLANG_VERSION(major,minor) (__clang_major__ > (major) || (__clang_major__ == (major) && __clang_minor__ >= (minor)))
		665
		666	#if __clang__ && defined __has_builtin
		667	#define ECB_CLANG_BUILTIN(x) __has_builtin (x)
		668	#else
		669	#define ECB_CLANG_BUILTIN(x) 0
		670	#endif
		671
		672	#if __clang__ && defined __has_extension
		673	#define ECB_CLANG_EXTENSION(x) __has_extension (x)
		674	#else
		675	#define ECB_CLANG_EXTENSION(x) 0
573	#endif	676	#endif
574		677
575	#define ECB_CPP (__cplusplus+0)	678	#define ECB_CPP (__cplusplus+0)
576	#define ECB_CPP11 (__cplusplus >= 201103L)	679	#define ECB_CPP11 (__cplusplus >= 201103L)
		680	#define ECB_CPP14 (__cplusplus >= 201402L)
		681	#define ECB_CPP17 (__cplusplus >= 201703L)
577		682
578	#if ECB_CPP	683	#if ECB_CPP
579	#define ECB_C 0	684	#define ECB_C 0
580	#define ECB_STDC_VERSION 0	685	#define ECB_STDC_VERSION 0
581	#else	686	#else
…		…
583	#define ECB_STDC_VERSION __STDC_VERSION__	688	#define ECB_STDC_VERSION __STDC_VERSION__
584	#endif	689	#endif
585		690
586	#define ECB_C99 (ECB_STDC_VERSION >= 199901L)	691	#define ECB_C99 (ECB_STDC_VERSION >= 199901L)
587	#define ECB_C11 (ECB_STDC_VERSION >= 201112L)	692	#define ECB_C11 (ECB_STDC_VERSION >= 201112L)
		693	#define ECB_C17 (ECB_STDC_VERSION >= 201710L)
588		694
589	#if ECB_CPP	695	#if ECB_CPP
590	#define ECB_EXTERN_C extern "C"	696	#define ECB_EXTERN_C extern "C"
591	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {	697	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {
592	#define ECB_EXTERN_C_END }	698	#define ECB_EXTERN_C_END }
…		…
607		713
608	#if ECB_NO_SMP	714	#if ECB_NO_SMP
609	#define ECB_MEMORY_FENCE do { } while (0)	715	#define ECB_MEMORY_FENCE do { } while (0)
610	#endif	716	#endif
611		717
		718	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/compiler_ref/compiler_builtins.html */
		719	#if __xlC__ && ECB_CPP
		720	#include <builtins.h>
		721	#endif
		722
		723	#if 1400 <= _MSC_VER
		724	#include <intrin.h> /* fence functions _ReadBarrier, also bit search functions _BitScanReverse */
		725	#endif
		726
612	#ifndef ECB_MEMORY_FENCE	727	#ifndef ECB_MEMORY_FENCE
613	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	728	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
		729	#define ECB_MEMORY_FENCE_RELAXED __asm__ __volatile__ ("" : : : "memory")
614	#if __i386 || __i386__	730	#if __i386 || __i386__
615	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")	731	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")
616	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")	732	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
617	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	733	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
618	#elif __amd64 || __amd64__ || __x86_64 || __x86_64__	734	#elif ECB_GCC_AMD64
619	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")	735	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")
620	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")	736	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
621	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	737	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
622	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__	738	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__
623	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")	739	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")
		740	#elif defined __ARM_ARCH_2__ \
		741	|| defined __ARM_ARCH_3__ || defined __ARM_ARCH_3M__ \
		742	|| defined __ARM_ARCH_4__ || defined __ARM_ARCH_4T__ \
		743	|| defined __ARM_ARCH_5__ || defined __ARM_ARCH_5E__ \
		744	|| defined __ARM_ARCH_5T__ || defined __ARM_ARCH_5TE__ \
		745	|| defined __ARM_ARCH_5TEJ__
		746	/* should not need any, unless running old code on newer cpu - arm doesn't support that */
624	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \	747	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \
625	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__	748	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__ \
		749	|| defined __ARM_ARCH_6T2__
626	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")	750	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")
627	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \	751	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \
628	|| defined __ARM_ARCH_7M__ || defined __ARM_ARCH_7R__	752	|| defined __ARM_ARCH_7R__ || defined __ARM_ARCH_7M__
629	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")	753	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")
630	#elif __aarch64__	754	#elif __aarch64__
631	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb ish" : : : "memory")	755	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb ish" : : : "memory")
632	#elif (__sparc || __sparc__) && !__sparcv8	756	#elif (__sparc || __sparc__) && !(__sparc_v8__ || defined __sparcv8)
633	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")	757	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")
634	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")	758	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")
635	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")	759	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")
636	#elif defined __s390__ || defined __s390x__	760	#elif defined __s390__ || defined __s390x__
637	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")	761	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")
…		…
660	#if ECB_GCC_VERSION(4,7)	784	#if ECB_GCC_VERSION(4,7)
661	/* see comment below (stdatomic.h) about the C11 memory model. */	785	/* see comment below (stdatomic.h) about the C11 memory model. */
662	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)	786	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)
663	#define ECB_MEMORY_FENCE_ACQUIRE __atomic_thread_fence (__ATOMIC_ACQUIRE)	787	#define ECB_MEMORY_FENCE_ACQUIRE __atomic_thread_fence (__ATOMIC_ACQUIRE)
664	#define ECB_MEMORY_FENCE_RELEASE __atomic_thread_fence (__ATOMIC_RELEASE)	788	#define ECB_MEMORY_FENCE_RELEASE __atomic_thread_fence (__ATOMIC_RELEASE)
		789	#define ECB_MEMORY_FENCE_RELAXED __atomic_thread_fence (__ATOMIC_RELAXED)
665		790
666	/* The __has_feature syntax from clang is so misdesigned that we cannot use it	791	#elif ECB_CLANG_EXTENSION(c_atomic)
667	* without risking compile time errors with other compilers. We *could*
668	* define our own ecb_clang_has_feature, but I just can't be bothered to work
669	* around this shit time and again.
670	* #elif defined __clang && __has_feature (cxx_atomic)
671	* // see comment below (stdatomic.h) about the C11 memory model.	792	/* see comment below (stdatomic.h) about the C11 memory model. */
672	* #define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)	793	#define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)
673	* #define ECB_MEMORY_FENCE_ACQUIRE __c11_atomic_thread_fence (__ATOMIC_ACQUIRE)	794	#define ECB_MEMORY_FENCE_ACQUIRE __c11_atomic_thread_fence (__ATOMIC_ACQUIRE)
674	* #define ECB_MEMORY_FENCE_RELEASE __c11_atomic_thread_fence (__ATOMIC_RELEASE)	795	#define ECB_MEMORY_FENCE_RELEASE __c11_atomic_thread_fence (__ATOMIC_RELEASE)
675	*/	796	#define ECB_MEMORY_FENCE_RELAXED __c11_atomic_thread_fence (__ATOMIC_RELAXED)
676		797
677	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__	798	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__
678	#define ECB_MEMORY_FENCE __sync_synchronize ()	799	#define ECB_MEMORY_FENCE __sync_synchronize ()
679	#elif _MSC_VER >= 1500 /* VC++ 2008 */	800	#elif _MSC_VER >= 1500 /* VC++ 2008 */
680	/* apparently, microsoft broke all the memory barrier stuff in Visual Studio 2008... */	801	/* apparently, microsoft broke all the memory barrier stuff in Visual Studio 2008... */
…		…
690	#elif defined _WIN32	811	#elif defined _WIN32
691	#include <WinNT.h>	812	#include <WinNT.h>
692	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */	813	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */
693	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	814	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
694	#include <mbarrier.h>	815	#include <mbarrier.h>
695	#define ECB_MEMORY_FENCE __machine_rw_barrier ()	816	#define ECB_MEMORY_FENCE __machine_rw_barrier ()
696	#define ECB_MEMORY_FENCE_ACQUIRE __machine_r_barrier ()	817	#define ECB_MEMORY_FENCE_ACQUIRE __machine_acq_barrier ()
697	#define ECB_MEMORY_FENCE_RELEASE __machine_w_barrier ()	818	#define ECB_MEMORY_FENCE_RELEASE __machine_rel_barrier ()
		819	#define ECB_MEMORY_FENCE_RELAXED __compiler_barrier ()
698	#elif __xlC__	820	#elif __xlC__
699	#define ECB_MEMORY_FENCE __sync ()	821	#define ECB_MEMORY_FENCE __sync ()
700	#endif	822	#endif
701	#endif	823	#endif
702		824
703	#ifndef ECB_MEMORY_FENCE	825	#ifndef ECB_MEMORY_FENCE
704	#if ECB_C11 && !defined __STDC_NO_ATOMICS__	826	#if ECB_C11 && !defined __STDC_NO_ATOMICS__
705	/* we assume that these memory fences work on all variables/all memory accesses, */	827	/* we assume that these memory fences work on all variables/all memory accesses, */
706	/* not just C11 atomics and atomic accesses */	828	/* not just C11 atomics and atomic accesses */
707	#include <stdatomic.h>	829	#include <stdatomic.h>
708	/* Unfortunately, neither gcc 4.7 nor clang 3.1 generate any instructions for */
709	/* any fence other than seq_cst, which isn't very efficient for us. */
710	/* Why that is, we don't know - either the C11 memory model is quite useless */
711	/* for most usages, or gcc and clang have a bug */
712	/* I *currently* lean towards the latter, and inefficiently implement */
713	/* all three of ecb's fences as a seq_cst fence */
714	/* Update, gcc-4.8 generates mfence for all c++ fences, but nothing */
715	/* for all __atomic_thread_fence's except seq_cst */
716	#define ECB_MEMORY_FENCE atomic_thread_fence (memory_order_seq_cst)	830	#define ECB_MEMORY_FENCE atomic_thread_fence (memory_order_seq_cst)
		831	#define ECB_MEMORY_FENCE_ACQUIRE atomic_thread_fence (memory_order_acquire)
		832	#define ECB_MEMORY_FENCE_RELEASE atomic_thread_fence (memory_order_release)
717	#endif	833	#endif
718	#endif	834	#endif
719		835
720	#ifndef ECB_MEMORY_FENCE	836	#ifndef ECB_MEMORY_FENCE
721	#if !ECB_AVOID_PTHREADS	837	#if !ECB_AVOID_PTHREADS
…		…
741		857
742	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE	858	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE
743	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	859	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
744	#endif	860	#endif
745		861
		862	#if !defined ECB_MEMORY_FENCE_RELAXED && defined ECB_MEMORY_FENCE
		863	#define ECB_MEMORY_FENCE_RELAXED ECB_MEMORY_FENCE /* very heavy-handed */
		864	#endif
		865
746	/*****************************************************************************/	866	/*****************************************************************************/
747		867
748	#if __cplusplus	868	#if ECB_CPP
749	#define ecb_inline static inline	869	#define ecb_inline static inline
750	#elif ECB_GCC_VERSION(2,5)	870	#elif ECB_GCC_VERSION(2,5)
751	#define ecb_inline static __inline__	871	#define ecb_inline static __inline__
752	#elif ECB_C99	872	#elif ECB_C99
753	#define ecb_inline static inline	873	#define ecb_inline static inline
…		…
767		887
768	#define ECB_CONCAT_(a, b) a ## b	888	#define ECB_CONCAT_(a, b) a ## b
769	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)	889	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)
770	#define ECB_STRINGIFY_(a) # a	890	#define ECB_STRINGIFY_(a) # a
771	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)	891	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)
		892	#define ECB_STRINGIFY_EXPR(expr) ((expr), ECB_STRINGIFY_ (expr))
772		893
773	#define ecb_function_ ecb_inline	894	#define ecb_function_ ecb_inline
774		895
775	#if ECB_GCC_VERSION(3,1)	896	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_VERSION(2,8)
776	#define ecb_attribute(attrlist) __attribute__(attrlist)	897	#define ecb_attribute(attrlist) __attribute__ (attrlist)
777	#define ecb_is_constant(expr) __builtin_constant_p (expr)
778	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))
779	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)
780	#else	898	#else
781	#define ecb_attribute(attrlist)	899	#define ecb_attribute(attrlist)
		900	#endif
782		901
		902	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_constant_p)
		903	#define ecb_is_constant(expr) __builtin_constant_p (expr)
		904	#else
783	/* possible C11 impl for integral types	905	/* possible C11 impl for integral types
784	typedef struct ecb_is_constant_struct ecb_is_constant_struct;	906	typedef struct ecb_is_constant_struct ecb_is_constant_struct;
785	#define ecb_is_constant(expr) _Generic ((1 ? (struct ecb_is_constant_struct *)0 : (void *)((expr) - (expr)), ecb_is_constant_struct *: 0, default: 1)) */	907	#define ecb_is_constant(expr) _Generic ((1 ? (struct ecb_is_constant_struct *)0 : (void *)((expr) - (expr)), ecb_is_constant_struct *: 0, default: 1)) */
786		908
787	#define ecb_is_constant(expr) 0	909	#define ecb_is_constant(expr) 0
		910	#endif
		911
		912	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_expect)
		913	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))
		914	#else
788	#define ecb_expect(expr,value) (expr)	915	#define ecb_expect(expr,value) (expr)
		916	#endif
		917
		918	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_prefetch)
		919	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)
		920	#else
789	#define ecb_prefetch(addr,rw,locality)	921	#define ecb_prefetch(addr,rw,locality)
790	#endif	922	#endif
791		923
792	/* no emulation for ecb_decltype */	924	/* no emulation for ecb_decltype */
793	#if ECB_GCC_VERSION(4,5)	925	#if ECB_CPP11
		926	// older implementations might have problems with decltype(x)::type, work around it
		927	template<class T> struct ecb_decltype_t { typedef T type; };
794	#define ecb_decltype(x) __decltype(x)	928	#define ecb_decltype(x) ecb_decltype_t<decltype (x)>::type
795	#elif ECB_GCC_VERSION(3,0)	929	#elif ECB_GCC_VERSION(3,0) || ECB_CLANG_VERSION(2,8)
796	#define ecb_decltype(x) __typeof(x)	930	#define ecb_decltype(x) __typeof__ (x)
797	#endif	931	#endif
798		932
		933	#if _MSC_VER >= 1300
		934	#define ecb_deprecated __declspec (deprecated)
		935	#else
		936	#define ecb_deprecated ecb_attribute ((__deprecated__))
		937	#endif
		938
		939	#if _MSC_VER >= 1500
		940	#define ecb_deprecated_message(msg) __declspec (deprecated (msg))
		941	#elif ECB_GCC_VERSION(4,5)
		942	#define ecb_deprecated_message(msg) ecb_attribute ((__deprecated__ (msg))
		943	#else
		944	#define ecb_deprecated_message(msg) ecb_deprecated
		945	#endif
		946
		947	#if _MSC_VER >= 1400
		948	#define ecb_noinline __declspec (noinline)
		949	#else
799	#define ecb_noinline ecb_attribute ((__noinline__))	950	#define ecb_noinline ecb_attribute ((__noinline__))
		951	#endif
		952
800	#define ecb_unused ecb_attribute ((__unused__))	953	#define ecb_unused ecb_attribute ((__unused__))
801	#define ecb_const ecb_attribute ((__const__))	954	#define ecb_const ecb_attribute ((__const__))
802	#define ecb_pure ecb_attribute ((__pure__))	955	#define ecb_pure ecb_attribute ((__pure__))
803		956
804	#if ECB_C11	957	#if ECB_C11 || __IBMC_NORETURN
		958	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/language_ref/noreturn.html */
805	#define ecb_noreturn _Noreturn	959	#define ecb_noreturn _Noreturn
		960	#elif ECB_CPP11
		961	#define ecb_noreturn [[noreturn]]
		962	#elif _MSC_VER >= 1200
		963	/* http://msdn.microsoft.com/en-us/library/k6ktzx3s.aspx */
		964	#define ecb_noreturn __declspec (noreturn)
806	#else	965	#else
807	#define ecb_noreturn ecb_attribute ((__noreturn__))	966	#define ecb_noreturn ecb_attribute ((__noreturn__))
808	#endif	967	#endif
809		968
810	#if ECB_GCC_VERSION(4,3)	969	#if ECB_GCC_VERSION(4,3)
…		…
825	/* for compatibility to the rest of the world */	984	/* for compatibility to the rest of the world */
826	#define ecb_likely(expr) ecb_expect_true (expr)	985	#define ecb_likely(expr) ecb_expect_true (expr)
827	#define ecb_unlikely(expr) ecb_expect_false (expr)	986	#define ecb_unlikely(expr) ecb_expect_false (expr)
828		987
829	/* count trailing zero bits and count # of one bits */	988	/* count trailing zero bits and count # of one bits */
830	#if ECB_GCC_VERSION(3,4)	989	#if ECB_GCC_VERSION(3,4) \
		990	|| (ECB_CLANG_BUILTIN(__builtin_clz) && ECB_CLANG_BUILTIN(__builtin_clzll) \
		991	&& ECB_CLANG_BUILTIN(__builtin_ctz) && ECB_CLANG_BUILTIN(__builtin_ctzll) \
		992	&& ECB_CLANG_BUILTIN(__builtin_popcount))
831	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */	993	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */
832	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)	994	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)
833	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)	995	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)
834	#define ecb_ctz32(x) __builtin_ctz (x)	996	#define ecb_ctz32(x) __builtin_ctz (x)
835	#define ecb_ctz64(x) __builtin_ctzll (x)	997	#define ecb_ctz64(x) __builtin_ctzll (x)
836	#define ecb_popcount32(x) __builtin_popcount (x)	998	#define ecb_popcount32(x) __builtin_popcount (x)
837	/* no popcountll */	999	/* no popcountll */
838	#else	1000	#else
839	ecb_function_ int ecb_ctz32 (uint32_t x) ecb_const;	1001	ecb_function_ ecb_const int ecb_ctz32 (uint32_t x);
840	ecb_function_ int	1002	ecb_function_ ecb_const int
841	ecb_ctz32 (uint32_t x)	1003	ecb_ctz32 (uint32_t x)
842	{	1004	{
		1005	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		1006	unsigned long r;
		1007	_BitScanForward (&r, x);
		1008	return (int)r;
		1009	#else
843	int r = 0;	1010	int r = 0;
844		1011
845	x &= ~x + 1; /* this isolates the lowest bit */	1012	x &= ~x + 1; /* this isolates the lowest bit */
846		1013
847	#if ECB_branchless_on_i386	1014	#if ECB_branchless_on_i386
…		…
857	if (x & 0xff00ff00) r += 8;	1024	if (x & 0xff00ff00) r += 8;
858	if (x & 0xffff0000) r += 16;	1025	if (x & 0xffff0000) r += 16;
859	#endif	1026	#endif
860		1027
861	return r;	1028	return r;
		1029	#endif
862	}	1030	}
863		1031
864	ecb_function_ int ecb_ctz64 (uint64_t x) ecb_const;	1032	ecb_function_ ecb_const int ecb_ctz64 (uint64_t x);
865	ecb_function_ int	1033	ecb_function_ ecb_const int
866	ecb_ctz64 (uint64_t x)	1034	ecb_ctz64 (uint64_t x)
867	{	1035	{
		1036	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1037	unsigned long r;
		1038	_BitScanForward64 (&r, x);
		1039	return (int)r;
		1040	#else
868	int shift = x & 0xffffffffU ? 0 : 32;	1041	int shift = x & 0xffffffff ? 0 : 32;
869	return ecb_ctz32 (x >> shift) + shift;	1042	return ecb_ctz32 (x >> shift) + shift;
		1043	#endif
870	}	1044	}
871		1045
872	ecb_function_ int ecb_popcount32 (uint32_t x) ecb_const;	1046	ecb_function_ ecb_const int ecb_popcount32 (uint32_t x);
873	ecb_function_ int	1047	ecb_function_ ecb_const int
874	ecb_popcount32 (uint32_t x)	1048	ecb_popcount32 (uint32_t x)
875	{	1049	{
876	x -= (x >> 1) & 0x55555555;	1050	x -= (x >> 1) & 0x55555555;
877	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);	1051	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);
878	x = ((x >> 4) + x) & 0x0f0f0f0f;	1052	x = ((x >> 4) + x) & 0x0f0f0f0f;
879	x *= 0x01010101;	1053	x *= 0x01010101;
880		1054
881	return x >> 24;	1055	return x >> 24;
882	}	1056	}
883		1057
884	ecb_function_ int ecb_ld32 (uint32_t x) ecb_const;	1058	ecb_function_ ecb_const int ecb_ld32 (uint32_t x);
885	ecb_function_ int ecb_ld32 (uint32_t x)	1059	ecb_function_ ecb_const int ecb_ld32 (uint32_t x)
886	{	1060	{
		1061	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		1062	unsigned long r;
		1063	_BitScanReverse (&r, x);
		1064	return (int)r;
		1065	#else
887	int r = 0;	1066	int r = 0;
888		1067
889	if (x >> 16) { x >>= 16; r += 16; }	1068	if (x >> 16) { x >>= 16; r += 16; }
890	if (x >> 8) { x >>= 8; r += 8; }	1069	if (x >> 8) { x >>= 8; r += 8; }
891	if (x >> 4) { x >>= 4; r += 4; }	1070	if (x >> 4) { x >>= 4; r += 4; }
892	if (x >> 2) { x >>= 2; r += 2; }	1071	if (x >> 2) { x >>= 2; r += 2; }
893	if (x >> 1) { r += 1; }	1072	if (x >> 1) { r += 1; }
894		1073
895	return r;	1074	return r;
		1075	#endif
896	}	1076	}
897		1077
898	ecb_function_ int ecb_ld64 (uint64_t x) ecb_const;	1078	ecb_function_ ecb_const int ecb_ld64 (uint64_t x);
899	ecb_function_ int ecb_ld64 (uint64_t x)	1079	ecb_function_ ecb_const int ecb_ld64 (uint64_t x)
900	{	1080	{
		1081	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1082	unsigned long r;
		1083	_BitScanReverse64 (&r, x);
		1084	return (int)r;
		1085	#else
901	int r = 0;	1086	int r = 0;
902		1087
903	if (x >> 32) { x >>= 32; r += 32; }	1088	if (x >> 32) { x >>= 32; r += 32; }
904		1089
905	return r + ecb_ld32 (x);	1090	return r + ecb_ld32 (x);
		1091	#endif
906	}	1092	}
907	#endif	1093	#endif
908		1094
909	ecb_function_ ecb_bool ecb_is_pot32 (uint32_t x) ecb_const;	1095	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x);
910	ecb_function_ ecb_bool ecb_is_pot32 (uint32_t x) { return !(x & (x - 1)); }	1096	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x) { return !(x & (x - 1)); }
911	ecb_function_ ecb_bool ecb_is_pot64 (uint64_t x) ecb_const;	1097	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x);
912	ecb_function_ ecb_bool ecb_is_pot64 (uint64_t x) { return !(x & (x - 1)); }	1098	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x) { return !(x & (x - 1)); }
913		1099
914	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x) ecb_const;	1100	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x);
915	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x)	1101	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x)
916	{	1102	{
917	return ( (x * 0x0802U & 0x22110U)	1103	return ( (x * 0x0802U & 0x22110U)
918	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;	1104	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;
919	}	1105	}
920		1106
921	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x) ecb_const;	1107	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x);
922	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x)	1108	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x)
923	{	1109	{
924	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);	1110	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);
925	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);	1111	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);
926	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);	1112	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);
927	x = ( x >> 8 ) | ( x << 8);	1113	x = ( x >> 8 ) | ( x << 8);
928		1114
929	return x;	1115	return x;
930	}	1116	}
931		1117
932	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x) ecb_const;	1118	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x);
933	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x)	1119	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x)
934	{	1120	{
935	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);	1121	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);
936	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);	1122	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);
937	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);	1123	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);
938	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);	1124	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);
…		…
941	return x;	1127	return x;
942	}	1128	}
943		1129
944	/* popcount64 is only available on 64 bit cpus as gcc builtin */	1130	/* popcount64 is only available on 64 bit cpus as gcc builtin */
945	/* so for this version we are lazy */	1131	/* so for this version we are lazy */
946	ecb_function_ int ecb_popcount64 (uint64_t x) ecb_const;	1132	ecb_function_ ecb_const int ecb_popcount64 (uint64_t x);
947	ecb_function_ int	1133	ecb_function_ ecb_const int
948	ecb_popcount64 (uint64_t x)	1134	ecb_popcount64 (uint64_t x)
949	{	1135	{
950	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);	1136	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);
951	}	1137	}
952		1138
953	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) ecb_const;	1139	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count);
954	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) ecb_const;	1140	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count);
955	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) ecb_const;	1141	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count);
956	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) ecb_const;	1142	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count);
957	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) ecb_const;	1143	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count);
958	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) ecb_const;	1144	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count);
959	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) ecb_const;	1145	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count);
960	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) ecb_const;	1146	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count);
961		1147
962	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }	1148	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }
963	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }	1149	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }
964	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }	1150	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }
965	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }	1151	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }
966	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }	1152	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }
967	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }	1153	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }
968	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }	1154	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }
969	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }	1155	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }
970		1156
971	#if ECB_GCC_VERSION(4,3)	1157	#if ECB_GCC_VERSION(4,3) || (ECB_CLANG_BUILTIN(__builtin_bswap32) && ECB_CLANG_BUILTIN(__builtin_bswap64))
		1158	#if ECB_GCC_VERSION(4,8) || ECB_CLANG_BUILTIN(__builtin_bswap16)
		1159	#define ecb_bswap16(x) __builtin_bswap16 (x)
		1160	#else
972	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)	1161	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)
		1162	#endif
973	#define ecb_bswap32(x) __builtin_bswap32 (x)	1163	#define ecb_bswap32(x) __builtin_bswap32 (x)
974	#define ecb_bswap64(x) __builtin_bswap64 (x)	1164	#define ecb_bswap64(x) __builtin_bswap64 (x)
		1165	#elif _MSC_VER
		1166	#include <stdlib.h>
		1167	#define ecb_bswap16(x) ((uint16_t)_byteswap_ushort ((uint16_t)(x)))
		1168	#define ecb_bswap32(x) ((uint32_t)_byteswap_ulong ((uint32_t)(x)))
		1169	#define ecb_bswap64(x) ((uint64_t)_byteswap_uint64 ((uint64_t)(x)))
975	#else	1170	#else
976	ecb_function_ uint16_t ecb_bswap16 (uint16_t x) ecb_const;	1171	ecb_function_ ecb_const uint16_t ecb_bswap16 (uint16_t x);
977	ecb_function_ uint16_t	1172	ecb_function_ ecb_const uint16_t
978	ecb_bswap16 (uint16_t x)	1173	ecb_bswap16 (uint16_t x)
979	{	1174	{
980	return ecb_rotl16 (x, 8);	1175	return ecb_rotl16 (x, 8);
981	}	1176	}
982		1177
983	ecb_function_ uint32_t ecb_bswap32 (uint32_t x) ecb_const;	1178	ecb_function_ ecb_const uint32_t ecb_bswap32 (uint32_t x);
984	ecb_function_ uint32_t	1179	ecb_function_ ecb_const uint32_t
985	ecb_bswap32 (uint32_t x)	1180	ecb_bswap32 (uint32_t x)
986	{	1181	{
987	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);	1182	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);
988	}	1183	}
989		1184
990	ecb_function_ uint64_t ecb_bswap64 (uint64_t x) ecb_const;	1185	ecb_function_ ecb_const uint64_t ecb_bswap64 (uint64_t x);
991	ecb_function_ uint64_t	1186	ecb_function_ ecb_const uint64_t
992	ecb_bswap64 (uint64_t x)	1187	ecb_bswap64 (uint64_t x)
993	{	1188	{
994	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);	1189	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);
995	}	1190	}
996	#endif	1191	#endif
997		1192
998	#if ECB_GCC_VERSION(4,5)	1193	#if ECB_GCC_VERSION(4,5) || ECB_CLANG_BUILTIN(__builtin_unreachable)
999	#define ecb_unreachable() __builtin_unreachable ()	1194	#define ecb_unreachable() __builtin_unreachable ()
1000	#else	1195	#else
1001	/* this seems to work fine, but gcc always emits a warning for it :/ */	1196	/* this seems to work fine, but gcc always emits a warning for it :/ */
1002	ecb_inline void ecb_unreachable (void) ecb_noreturn;	1197	ecb_inline ecb_noreturn void ecb_unreachable (void);
1003	ecb_inline void ecb_unreachable (void) { }	1198	ecb_inline ecb_noreturn void ecb_unreachable (void) { }
1004	#endif	1199	#endif
1005		1200
1006	/* try to tell the compiler that some condition is definitely true */	1201	/* try to tell the compiler that some condition is definitely true */
1007	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0	1202	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0
1008		1203
1009	ecb_inline unsigned char ecb_byteorder_helper (void) ecb_const;	1204	ecb_inline ecb_const uint32_t ecb_byteorder_helper (void);
1010	ecb_inline unsigned char	1205	ecb_inline ecb_const uint32_t
1011	ecb_byteorder_helper (void)	1206	ecb_byteorder_helper (void)
1012	{	1207	{
1013	/* the union code still generates code under pressure in gcc, */	1208	/* the union code still generates code under pressure in gcc, */
1014	/* but less than using pointers, and always seems to */	1209	/* but less than using pointers, and always seems to */
1015	/* successfully return a constant. */	1210	/* successfully return a constant. */
1016	/* the reason why we have this horrible preprocessor mess */	1211	/* the reason why we have this horrible preprocessor mess */
1017	/* is to avoid it in all cases, at least on common architectures */	1212	/* is to avoid it in all cases, at least on common architectures */
1018	/* or when using a recent enough gcc version (>= 4.6) */	1213	/* or when using a recent enough gcc version (>= 4.6) */
1019	#if __i386 || __i386__ || _M_X86 || __amd64 || __amd64__ || _M_X64
1020	return 0x44;
1021	#elif __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_LITTLE_ENDIAN__	1214	#if (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_LITTLE_ENDIAN__) \
		1215	|| ((__i386 || __i386__ || _M_IX86 || ECB_GCC_AMD64 || ECB_MSVC_AMD64) && !__VOS__)
		1216	#define ECB_LITTLE_ENDIAN 1
1022	return 0x44;	1217	return 0x44332211;
1023	#elif __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__	1218	#elif (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__) \
		1219	|| ((__AARCH64EB__ || __MIPSEB__ || __ARMEB__) && !__VOS__)
		1220	#define ECB_BIG_ENDIAN 1
1024	return 0x11;	1221	return 0x11223344;
1025	#else	1222	#else
1026	union	1223	union
1027	{	1224	{
		1225	uint8_t c[4];
1028	uint32_t i;	1226	uint32_t u;
1029	uint8_t c;
1030	} u = { 0x11223344 };	1227	} u = { 0x11, 0x22, 0x33, 0x44 };
1031	return u.c;	1228	return u.u;
1032	#endif	1229	#endif
1033	}	1230	}
1034		1231
1035	ecb_inline ecb_bool ecb_big_endian (void) ecb_const;	1232	ecb_inline ecb_const ecb_bool ecb_big_endian (void);
1036	ecb_inline ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11; }	1233	ecb_inline ecb_const ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11223344; }
1037	ecb_inline ecb_bool ecb_little_endian (void) ecb_const;	1234	ecb_inline ecb_const ecb_bool ecb_little_endian (void);
1038	ecb_inline ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44; }	1235	ecb_inline ecb_const ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44332211; }
1039		1236
1040	#if ECB_GCC_VERSION(3,0) || ECB_C99	1237	#if ECB_GCC_VERSION(3,0) || ECB_C99
1041	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))	1238	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))
1042	#else	1239	#else
1043	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))	1240	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))
1044	#endif	1241	#endif
1045		1242
1046	#if __cplusplus	1243	#if ECB_CPP
1047	template<typename T>	1244	template<typename T>
1048	static inline T ecb_div_rd (T val, T div)	1245	static inline T ecb_div_rd (T val, T div)
1049	{	1246	{
1050	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;	1247	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;
1051	}	1248	}
…		…
1068	}	1265	}
1069	#else	1266	#else
1070	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))	1267	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))
1071	#endif	1268	#endif
1072		1269
		1270	ecb_function_ ecb_const uint32_t ecb_binary16_to_binary32 (uint32_t x);
		1271	ecb_function_ ecb_const uint32_t
		1272	ecb_binary16_to_binary32 (uint32_t x)
		1273	{
		1274	unsigned int s = (x & 0x8000) << (31 - 15);
		1275	int e = (x >> 10) & 0x001f;
		1276	unsigned int m = x & 0x03ff;
		1277
		1278	if (ecb_expect_false (e == 31))
		1279	/* infinity or NaN */
		1280	e = 255 - (127 - 15);
		1281	else if (ecb_expect_false (!e))
		1282	{
		1283	if (ecb_expect_true (!m))
		1284	/* zero, handled by code below by forcing e to 0 */
		1285	e = 0 - (127 - 15);
		1286	else
		1287	{
		1288	/* subnormal, renormalise */
		1289	unsigned int s = 10 - ecb_ld32 (m);
		1290
		1291	m = (m << s) & 0x3ff; /* mask implicit bit */
		1292	e -= s - 1;
		1293	}
		1294	}
		1295
		1296	/* e and m now are normalised, or zero, (or inf or nan) */
		1297	e += 127 - 15;
		1298
		1299	return s | (e << 23) | (m << (23 - 10));
		1300	}
		1301
		1302	ecb_function_ ecb_const uint16_t ecb_binary32_to_binary16 (uint32_t x);
		1303	ecb_function_ ecb_const uint16_t
		1304	ecb_binary32_to_binary16 (uint32_t x)
		1305	{
		1306	unsigned int s = (x >> 16) & 0x00008000; /* sign bit, the easy part */
		1307	unsigned int e = ((x >> 23) & 0x000000ff) - (127 - 15); /* the desired exponent */
		1308	unsigned int m = x & 0x007fffff;
		1309
		1310	x &= 0x7fffffff;
		1311
		1312	/* if it's within range of binary16 normals, use fast path */
		1313	if (ecb_expect_true (0x38800000 <= x && x <= 0x477fefff))
		1314	{
		1315	/* mantissa round-to-even */
		1316	m += 0x00000fff + ((m >> (23 - 10)) & 1);
		1317
		1318	/* handle overflow */
		1319	if (ecb_expect_false (m >= 0x00800000))
		1320	{
		1321	m >>= 1;
		1322	e += 1;
		1323	}
		1324
		1325	return s | (e << 10) | (m >> (23 - 10));
		1326	}
		1327
		1328	/* handle large numbers and infinity */
		1329	if (ecb_expect_true (0x477fefff < x && x <= 0x7f800000))
		1330	return s | 0x7c00;
		1331
		1332	/* handle zero, subnormals and small numbers */
		1333	if (ecb_expect_true (x < 0x38800000))
		1334	{
		1335	/* zero */
		1336	if (ecb_expect_true (!x))
		1337	return s;
		1338
		1339	/* handle subnormals */
		1340
		1341	/* too small, will be zero */
		1342	if (e < (14 - 24)) /* might not be sharp, but is good enough */
		1343	return s;
		1344
		1345	m |= 0x00800000; /* make implicit bit explicit */
		1346
		1347	/* very tricky - we need to round to the nearest e (+10) bit value */
		1348	{
		1349	unsigned int bits = 14 - e;
		1350	unsigned int half = (1 << (bits - 1)) - 1;
		1351	unsigned int even = (m >> bits) & 1;
		1352
		1353	/* if this overflows, we will end up with a normalised number */
		1354	m = (m + half + even) >> bits;
		1355	}
		1356
		1357	return s | m;
		1358	}
		1359
		1360	/* handle NaNs, preserve leftmost nan bits, but make sure we don't turn them into infinities */
		1361	m >>= 13;
		1362
		1363	return s | 0x7c00 | m | !m;
		1364	}
		1365
1073	/*******************************************************************************/	1366	/*******************************************************************************/
1074	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */	1367	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */
1075		1368
1076	/* basically, everything uses "ieee pure-endian" floating point numbers */	1369	/* basically, everything uses "ieee pure-endian" floating point numbers */
1077	/* the only noteworthy exception is ancient armle, which uses order 43218765 */	1370	/* the only noteworthy exception is ancient armle, which uses order 43218765 */
1078	#if 0 \	1371	#if 0 \
1079	|| __i386 || __i386__ \	1372	|| __i386 || __i386__ \
1080	|| __amd64 || __amd64__ || __x86_64 || __x86_64__ \	1373	|| ECB_GCC_AMD64 \
1081	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \	1374	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \
1082	|| defined __arm__ && defined __ARM_EABI__ \
1083	|| defined __s390__ || defined __s390x__ \	1375	|| defined __s390__ || defined __s390x__ \
1084	|| defined __mips__ \	1376	|| defined __mips__ \
1085	|| defined __alpha__ \	1377	|| defined __alpha__ \
1086	|| defined __hppa__ \	1378	|| defined __hppa__ \
1087	|| defined __ia64__ \	1379	|| defined __ia64__ \
1088	|| defined __m68k__ \	1380	|| defined __m68k__ \
1089	|| defined __m88k__ \	1381	|| defined __m88k__ \
1090	|| defined __sh__ \	1382	|| defined __sh__ \
1091	|| defined _M_IX86 || defined _M_AMD64 || defined _M_IA64 \	1383	|| defined _M_IX86 || defined ECB_MSVC_AMD64 || defined _M_IA64 \
1092	|| (defined __arm__ && (defined __ARM_EABI__ || defined __EABI__ || defined __VFP_FP__ || defined _WIN32_WCE || defined __ANDROID__))	1384	|| (defined __arm__ && (defined __ARM_EABI__ || defined __EABI__ || defined __VFP_FP__ || defined _WIN32_WCE || defined __ANDROID__)) \
		1385	|| defined __aarch64__
1093	#define ECB_STDFP 1	1386	#define ECB_STDFP 1
1094	#include <string.h> /* for memcpy */	1387	#include <string.h> /* for memcpy */
1095	#else	1388	#else
1096	#define ECB_STDFP 0	1389	#define ECB_STDFP 0
1097	#endif	1390	#endif
…		…
1111	#define ECB_NAN NAN	1404	#define ECB_NAN NAN
1112	#else	1405	#else
1113	#define ECB_NAN ECB_INFINITY	1406	#define ECB_NAN ECB_INFINITY
1114	#endif	1407	#endif
1115		1408
1116	/* converts an ieee half/binary16 to a float */	1409	#if ECB_C99 || _XOPEN_VERSION >= 600 || _POSIX_VERSION >= 200112L
1117	ecb_function_ float ecb_binary16_to_float (uint16_t x) ecb_const;	1410	#define ecb_ldexpf(x,e) ldexpf ((x), (e))
1118	ecb_function_ float	1411	#define ecb_frexpf(x,e) frexpf ((x), (e))
1119	ecb_binary16_to_float (uint16_t x)	1412	#else
1120	{	1413	#define ecb_ldexpf(x,e) (float) ldexp ((double) (x), (e))
1121	int e = (x >> 10) & 0x1f;	1414	#define ecb_frexpf(x,e) (float) frexp ((double) (x), (e))
1122	int m = x & 0x3ff;	1415	#endif
1123	float r;
1124
1125	if (!e ) r = ldexpf (m , -24);
1126	else if (e != 31) r = ldexpf (m + 0x400, e - 25);
1127	else if (m ) r = ECB_NAN;
1128	else r = ECB_INFINITY;
1129
1130	return x & 0x8000 ? -r : r;
1131	}
1132		1416
1133	/* convert a float to ieee single/binary32 */	1417	/* convert a float to ieee single/binary32 */
1134	ecb_function_ uint32_t ecb_float_to_binary32 (float x) ecb_const;	1418	ecb_function_ ecb_const uint32_t ecb_float_to_binary32 (float x);
1135	ecb_function_ uint32_t	1419	ecb_function_ ecb_const uint32_t
1136	ecb_float_to_binary32 (float x)	1420	ecb_float_to_binary32 (float x)
1137	{	1421	{
1138	uint32_t r;	1422	uint32_t r;
1139		1423
1140	#if ECB_STDFP	1424	#if ECB_STDFP
…		…
1147	if (x == 0e0f ) return 0x00000000U;	1431	if (x == 0e0f ) return 0x00000000U;
1148	if (x > +3.40282346638528860e+38f) return 0x7f800000U;	1432	if (x > +3.40282346638528860e+38f) return 0x7f800000U;
1149	if (x < -3.40282346638528860e+38f) return 0xff800000U;	1433	if (x < -3.40282346638528860e+38f) return 0xff800000U;
1150	if (x != x ) return 0x7fbfffffU;	1434	if (x != x ) return 0x7fbfffffU;
1151		1435
1152	m = frexpf (x, &e) * 0x1000000U;	1436	m = ecb_frexpf (x, &e) * 0x1000000U;
1153		1437
1154	r = m & 0x80000000U;	1438	r = m & 0x80000000U;
1155		1439
1156	if (r)	1440	if (r)
1157	m = -m;	1441	m = -m;
…		…
1169		1453
1170	return r;	1454	return r;
1171	}	1455	}
1172		1456
1173	/* converts an ieee single/binary32 to a float */	1457	/* converts an ieee single/binary32 to a float */
1174	ecb_function_ float ecb_binary32_to_float (uint32_t x) ecb_const;	1458	ecb_function_ ecb_const float ecb_binary32_to_float (uint32_t x);
1175	ecb_function_ float	1459	ecb_function_ ecb_const float
1176	ecb_binary32_to_float (uint32_t x)	1460	ecb_binary32_to_float (uint32_t x)
1177	{	1461	{
1178	float r;	1462	float r;
1179		1463
1180	#if ECB_STDFP	1464	#if ECB_STDFP
…		…
1190	x |= 0x800000U;	1474	x |= 0x800000U;
1191	else	1475	else
1192	e = 1;	1476	e = 1;
1193		1477
1194	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */	1478	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */
1195	r = ldexpf (x * (0.5f / 0x800000U), e - 126);	1479	r = ecb_ldexpf (x * (0.5f / 0x800000U), e - 126);
1196		1480
1197	r = neg ? -r : r;	1481	r = neg ? -r : r;
1198	#endif	1482	#endif
1199		1483
1200	return r;	1484	return r;
1201	}	1485	}
1202		1486
1203	/* convert a double to ieee double/binary64 */	1487	/* convert a double to ieee double/binary64 */
1204	ecb_function_ uint64_t ecb_double_to_binary64 (double x) ecb_const;	1488	ecb_function_ ecb_const uint64_t ecb_double_to_binary64 (double x);
1205	ecb_function_ uint64_t	1489	ecb_function_ ecb_const uint64_t
1206	ecb_double_to_binary64 (double x)	1490	ecb_double_to_binary64 (double x)
1207	{	1491	{
1208	uint64_t r;	1492	uint64_t r;
1209		1493
1210	#if ECB_STDFP	1494	#if ECB_STDFP
…		…
1239		1523
1240	return r;	1524	return r;
1241	}	1525	}
1242		1526
1243	/* converts an ieee double/binary64 to a double */	1527	/* converts an ieee double/binary64 to a double */
1244	ecb_function_ double ecb_binary64_to_double (uint64_t x) ecb_const;	1528	ecb_function_ ecb_const double ecb_binary64_to_double (uint64_t x);
1245	ecb_function_ double	1529	ecb_function_ ecb_const double
1246	ecb_binary64_to_double (uint64_t x)	1530	ecb_binary64_to_double (uint64_t x)
1247	{	1531	{
1248	double r;	1532	double r;
1249		1533
1250	#if ECB_STDFP	1534	#if ECB_STDFP
…		…
1268	#endif	1552	#endif
1269		1553
1270	return r;	1554	return r;
1271	}	1555	}
1272		1556
		1557	/* convert a float to ieee half/binary16 */
		1558	ecb_function_ ecb_const uint16_t ecb_float_to_binary16 (float x);
		1559	ecb_function_ ecb_const uint16_t
		1560	ecb_float_to_binary16 (float x)
		1561	{
		1562	return ecb_binary32_to_binary16 (ecb_float_to_binary32 (x));
		1563	}
		1564
		1565	/* convert an ieee half/binary16 to float */
		1566	ecb_function_ ecb_const float ecb_binary16_to_float (uint16_t x);
		1567	ecb_function_ ecb_const float
		1568	ecb_binary16_to_float (uint16_t x)
		1569	{
		1570	return ecb_binary32_to_float (ecb_binary16_to_binary32 (x));
		1571	}
		1572
1273	#endif	1573	#endif
1274		1574
1275	#endif	1575	#endif
1276		1576
1277	/* ECB.H END */	1577	/* ECB.H END */
1278		1578
1279	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS	1579	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS
1280	/* if your architecture doesn't need memory fences, e.g. because it is	1580	/* if your architecture doesn't need memory fences, e.g. because it is
1281	* single-cpu/core, or if you use libev in a project that doesn't use libev	1581	* single-cpu/core, or if you use libev in a project that doesn't use libev
1282	* from multiple threads, then you can define ECB_AVOID_PTHREADS when compiling	1582	* from multiple threads, then you can define ECB_NO_THREADS when compiling
1283	* libev, in which cases the memory fences become nops.	1583	* libev, in which cases the memory fences become nops.
1284	* alternatively, you can remove this #error and link against libpthread,	1584	* alternatively, you can remove this #error and link against libpthread,
1285	* which will then provide the memory fences.	1585	* which will then provide the memory fences.
1286	*/	1586	*/
1287	# error "memory fences not defined for your architecture, please report"	1587	# error "memory fences not defined for your architecture, please report"
…		…
1291	# define ECB_MEMORY_FENCE do { } while (0)	1591	# define ECB_MEMORY_FENCE do { } while (0)
1292	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE	1592	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE
1293	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	1593	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
1294	#endif	1594	#endif
1295		1595
1296	#define expect_false(cond) ecb_expect_false (cond)
1297	#define expect_true(cond) ecb_expect_true (cond)
1298	#define noinline ecb_noinline
1299
1300	#define inline_size ecb_inline	1596	#define inline_size ecb_inline
1301		1597
1302	#if EV_FEATURE_CODE	1598	#if EV_FEATURE_CODE
1303	# define inline_speed ecb_inline	1599	# define inline_speed ecb_inline
1304	#else	1600	#else
1305	# define inline_speed static noinline	1601	# define inline_speed ecb_noinline static
1306	#endif	1602	#endif
		1603
		1604	/*****************************************************************************/
		1605	/* raw syscall wrappers */
		1606
		1607	#if EV_NEED_SYSCALL
		1608
		1609	#include <sys/syscall.h>
		1610
		1611	/*
		1612	* define some syscall wrappers for common architectures
		1613	* this is mostly for nice looks during debugging, not performance.
		1614	* our syscalls return < 0, not == -1, on error. which is good
		1615	* enough for linux aio.
		1616	* TODO: arm is also common nowadays, maybe even mips and x86
		1617	* TODO: after implementing this, it suddenly looks like overkill, but its hard to remove...
		1618	*/
		1619	#if __GNUC__ && __linux && ECB_AMD64 && !defined __OPTIMIZE_SIZE__
		1620	/* the costly errno access probably kills this for size optimisation */
		1621
		1622	#define ev_syscall(nr,narg,arg1,arg2,arg3,arg4,arg5,arg6) \
		1623	({ \
		1624	long res; \
		1625	register unsigned long r6 __asm__ ("r9" ); \
		1626	register unsigned long r5 __asm__ ("r8" ); \
		1627	register unsigned long r4 __asm__ ("r10"); \
		1628	register unsigned long r3 __asm__ ("rdx"); \
		1629	register unsigned long r2 __asm__ ("rsi"); \
		1630	register unsigned long r1 __asm__ ("rdi"); \
		1631	if (narg >= 6) r6 = (unsigned long)(arg6); \
		1632	if (narg >= 5) r5 = (unsigned long)(arg5); \
		1633	if (narg >= 4) r4 = (unsigned long)(arg4); \
		1634	if (narg >= 3) r3 = (unsigned long)(arg3); \
		1635	if (narg >= 2) r2 = (unsigned long)(arg2); \
		1636	if (narg >= 1) r1 = (unsigned long)(arg1); \
		1637	__asm__ __volatile__ ( \
		1638	"syscall\n\t" \
		1639	: "=a" (res) \
		1640	: "0" (nr), "r" (r1), "r" (r2), "r" (r3), "r" (r4), "r" (r5) \
		1641	: "cc", "r11", "cx", "memory"); \
		1642	errno = -res; \
		1643	res; \
		1644	})
		1645
		1646	#endif
		1647
		1648	#ifdef ev_syscall
		1649	#define ev_syscall0(nr) ev_syscall (nr, 0, 0, 0, 0, 0, 0, 0)
		1650	#define ev_syscall1(nr,arg1) ev_syscall (nr, 1, arg1, 0, 0, 0, 0, 0)
		1651	#define ev_syscall2(nr,arg1,arg2) ev_syscall (nr, 2, arg1, arg2, 0, 0, 0, 0)
		1652	#define ev_syscall3(nr,arg1,arg2,arg3) ev_syscall (nr, 3, arg1, arg2, arg3, 0, 0, 0)
		1653	#define ev_syscall4(nr,arg1,arg2,arg3,arg4) ev_syscall (nr, 3, arg1, arg2, arg3, arg4, 0, 0)
		1654	#define ev_syscall5(nr,arg1,arg2,arg3,arg4,arg5) ev_syscall (nr, 5, arg1, arg2, arg3, arg4, arg5, 0)
		1655	#define ev_syscall6(nr,arg1,arg2,arg3,arg4,arg5,arg6) ev_syscall (nr, 6, arg1, arg2, arg3, arg4, arg5,arg6)
		1656	#else
		1657	#define ev_syscall0(nr) syscall (nr)
		1658	#define ev_syscall1(nr,arg1) syscall (nr, arg1)
		1659	#define ev_syscall2(nr,arg1,arg2) syscall (nr, arg1, arg2)
		1660	#define ev_syscall3(nr,arg1,arg2,arg3) syscall (nr, arg1, arg2, arg3)
		1661	#define ev_syscall4(nr,arg1,arg2,arg3,arg4) syscall (nr, arg1, arg2, arg3, arg4)
		1662	#define ev_syscall5(nr,arg1,arg2,arg3,arg4,arg5) syscall (nr, arg1, arg2, arg3, arg4, arg5)
		1663	#define ev_syscall6(nr,arg1,arg2,arg3,arg4,arg5,arg6) syscall (nr, arg1, arg2, arg3, arg4, arg5,arg6)
		1664	#endif
		1665
		1666	#endif
		1667
		1668	/*****************************************************************************/
1307		1669
1308	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)	1670	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)
1309		1671
1310	#if EV_MINPRI == EV_MAXPRI	1672	#if EV_MINPRI == EV_MAXPRI
1311	# define ABSPRI(w) (((W)w), 0)	1673	# define ABSPRI(w) (((W)w), 0)
1312	#else	1674	#else
1313	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)	1675	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)
1314	#endif	1676	#endif
1315		1677
1316	#define EMPTY /* required for microsofts broken pseudo-c compiler */	1678	#define EMPTY /* required for microsofts broken pseudo-c compiler */
1317	#define EMPTY2(a,b) /* used to suppress some warnings */
1318		1679
1319	typedef ev_watcher *W;	1680	typedef ev_watcher *W;
1320	typedef ev_watcher_list *WL;	1681	typedef ev_watcher_list *WL;
1321	typedef ev_watcher_time *WT;	1682	typedef ev_watcher_time *WT;
1322		1683
…		…
1347	# include "ev_win32.c"	1708	# include "ev_win32.c"
1348	#endif	1709	#endif
1349		1710
1350	/*****************************************************************************/	1711	/*****************************************************************************/
1351		1712
		1713	#if EV_USE_LINUXAIO
		1714	# include <linux/aio_abi.h> /* probably only needed for aio_context_t */
		1715	#endif
		1716
1352	/* define a suitable floor function (only used by periodics atm) */	1717	/* define a suitable floor function (only used by periodics atm) */
1353		1718
1354	#if EV_USE_FLOOR	1719	#if EV_USE_FLOOR
1355	# include <math.h>	1720	# include <math.h>
1356	# define ev_floor(v) floor (v)	1721	# define ev_floor(v) floor (v)
1357	#else	1722	#else
1358		1723
1359	#include <float.h>	1724	#include <float.h>
1360		1725
1361	/* a floor() replacement function, should be independent of ev_tstamp type */	1726	/* a floor() replacement function, should be independent of ev_tstamp type */
		1727	ecb_noinline
1362	static ev_tstamp noinline	1728	static ev_tstamp
1363	ev_floor (ev_tstamp v)	1729	ev_floor (ev_tstamp v)
1364	{	1730	{
1365	/* the choice of shift factor is not terribly important */	1731	/* the choice of shift factor is not terribly important */
1366	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */	1732	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */
1367	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;	1733	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;
1368	#else	1734	#else
1369	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;	1735	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;
1370	#endif	1736	#endif
1371		1737
		1738	/* special treatment for negative arguments */
		1739	if (ecb_expect_false (v < 0.))
		1740	{
		1741	ev_tstamp f = -ev_floor (-v);
		1742
		1743	return f - (f == v ? 0 : 1);
		1744	}
		1745
1372	/* argument too large for an unsigned long? */	1746	/* argument too large for an unsigned long? then reduce it */
1373	if (expect_false (v >= shift))	1747	if (ecb_expect_false (v >= shift))
1374	{	1748	{
1375	ev_tstamp f;	1749	ev_tstamp f;
1376		1750
1377	if (v == v - 1.)	1751	if (v == v - 1.)
1378	return v; /* very large number */	1752	return v; /* very large numbers are assumed to be integer */
1379		1753
1380	f = shift * ev_floor (v * (1. / shift));	1754	f = shift * ev_floor (v * (1. / shift));
1381	return f + ev_floor (v - f);	1755	return f + ev_floor (v - f);
1382	}	1756	}
1383		1757
1384	/* special treatment for negative args? */
1385	if (expect_false (v < 0.))
1386	{
1387	ev_tstamp f = -ev_floor (-v);
1388
1389	return f - (f == v ? 0 : 1);
1390	}
1391
1392	/* fits into an unsigned long */	1758	/* fits into an unsigned long */
1393	return (unsigned long)v;	1759	return (unsigned long)v;
1394	}	1760	}
1395		1761
1396	#endif	1762	#endif
…		…
1399		1765
1400	#ifdef __linux	1766	#ifdef __linux
1401	# include <sys/utsname.h>	1767	# include <sys/utsname.h>
1402	#endif	1768	#endif
1403		1769
1404	static unsigned int noinline ecb_cold	1770	ecb_noinline ecb_cold
		1771	static unsigned int
1405	ev_linux_version (void)	1772	ev_linux_version (void)
1406	{	1773	{
1407	#ifdef __linux	1774	#ifdef __linux
1408	unsigned int v = 0;	1775	unsigned int v = 0;
1409	struct utsname buf;	1776	struct utsname buf;
…		…
1438	}	1805	}
1439		1806
1440	/*****************************************************************************/	1807	/*****************************************************************************/
1441		1808
1442	#if EV_AVOID_STDIO	1809	#if EV_AVOID_STDIO
1443	static void noinline ecb_cold	1810	ecb_noinline ecb_cold
		1811	static void
1444	ev_printerr (const char *msg)	1812	ev_printerr (const char *msg)
1445	{	1813	{
1446	write (STDERR_FILENO, msg, strlen (msg));	1814	write (STDERR_FILENO, msg, strlen (msg));
1447	}	1815	}
1448	#endif	1816	#endif
1449		1817
1450	static void (*syserr_cb)(const char *msg) EV_THROW;	1818	static void (*syserr_cb)(const char *msg) EV_NOEXCEPT;
1451		1819
1452	void ecb_cold	1820	ecb_cold
		1821	void
1453	ev_set_syserr_cb (void (*cb)(const char *msg) EV_THROW) EV_THROW	1822	ev_set_syserr_cb (void (*cb)(const char *msg) EV_NOEXCEPT) EV_NOEXCEPT
1454	{	1823	{
1455	syserr_cb = cb;	1824	syserr_cb = cb;
1456	}	1825	}
1457		1826
1458	static void noinline ecb_cold	1827	ecb_noinline ecb_cold
		1828	static void
1459	ev_syserr (const char *msg)	1829	ev_syserr (const char *msg)
1460	{	1830	{
1461	if (!msg)	1831	if (!msg)
1462	msg = "(libev) system error";	1832	msg = "(libev) system error";
1463		1833
…		…
1476	abort ();	1846	abort ();
1477	}	1847	}
1478	}	1848	}
1479		1849
1480	static void *	1850	static void *
1481	ev_realloc_emul (void *ptr, long size) EV_THROW	1851	ev_realloc_emul (void *ptr, long size) EV_NOEXCEPT
1482	{	1852	{
1483	/* some systems, notably openbsd and darwin, fail to properly	1853	/* some systems, notably openbsd and darwin, fail to properly
1484	* implement realloc (x, 0) (as required by both ansi c-89 and	1854	* implement realloc (x, 0) (as required by both ansi c-89 and
1485	* the single unix specification, so work around them here.	1855	* the single unix specification, so work around them here.
1486	* recently, also (at least) fedora and debian started breaking it,	1856	* recently, also (at least) fedora and debian started breaking it,
…		…
1492		1862
1493	free (ptr);	1863	free (ptr);
1494	return 0;	1864	return 0;
1495	}	1865	}
1496		1866
1497	static void *(*alloc)(void *ptr, long size) EV_THROW = ev_realloc_emul;	1867	static void *(*alloc)(void *ptr, long size) EV_NOEXCEPT = ev_realloc_emul;
1498		1868
1499	void ecb_cold	1869	ecb_cold
		1870	void
1500	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_THROW) EV_THROW	1871	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_NOEXCEPT) EV_NOEXCEPT
1501	{	1872	{
1502	alloc = cb;	1873	alloc = cb;
1503	}	1874	}
1504		1875
1505	inline_speed void *	1876	inline_speed void *
…		…
1532	typedef struct	1903	typedef struct
1533	{	1904	{
1534	WL head;	1905	WL head;
1535	unsigned char events; /* the events watched for */	1906	unsigned char events; /* the events watched for */
1536	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */	1907	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */
1537	unsigned char emask; /* the epoll backend stores the actual kernel mask in here */	1908	unsigned char emask; /* some backends store the actual kernel mask in here */
1538	unsigned char unused;	1909	unsigned char eflags; /* flags field for use by backends */
1539	#if EV_USE_EPOLL	1910	#if EV_USE_EPOLL
1540	unsigned int egen; /* generation counter to counter epoll bugs */	1911	unsigned int egen; /* generation counter to counter epoll bugs */
1541	#endif	1912	#endif
1542	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP	1913	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP
1543	SOCKET handle;	1914	SOCKET handle;
…		…
1597	static struct ev_loop default_loop_struct;	1968	static struct ev_loop default_loop_struct;
1598	EV_API_DECL struct ev_loop *ev_default_loop_ptr = 0; /* needs to be initialised to make it a definition despite extern */	1969	EV_API_DECL struct ev_loop *ev_default_loop_ptr = 0; /* needs to be initialised to make it a definition despite extern */
1599		1970
1600	#else	1971	#else
1601		1972
1602	EV_API_DECL ev_tstamp ev_rt_now = 0; /* needs to be initialised to make it a definition despite extern */	1973	EV_API_DECL ev_tstamp ev_rt_now = EV_TS_CONST (0.); /* needs to be initialised to make it a definition despite extern */
1603	#define VAR(name,decl) static decl;	1974	#define VAR(name,decl) static decl;
1604	#include "ev_vars.h"	1975	#include "ev_vars.h"
1605	#undef VAR	1976	#undef VAR
1606		1977
1607	static int ev_default_loop_ptr;	1978	static int ev_default_loop_ptr;
1608		1979
1609	#endif	1980	#endif
1610		1981
1611	#if EV_FEATURE_API	1982	#if EV_FEATURE_API
1612	# define EV_RELEASE_CB if (expect_false (release_cb)) release_cb (EV_A)	1983	# define EV_RELEASE_CB if (ecb_expect_false (release_cb)) release_cb (EV_A)
1613	# define EV_ACQUIRE_CB if (expect_false (acquire_cb)) acquire_cb (EV_A)	1984	# define EV_ACQUIRE_CB if (ecb_expect_false (acquire_cb)) acquire_cb (EV_A)
1614	# define EV_INVOKE_PENDING invoke_cb (EV_A)	1985	# define EV_INVOKE_PENDING invoke_cb (EV_A)
1615	#else	1986	#else
1616	# define EV_RELEASE_CB (void)0	1987	# define EV_RELEASE_CB (void)0
1617	# define EV_ACQUIRE_CB (void)0	1988	# define EV_ACQUIRE_CB (void)0
1618	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)	1989	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)
…		…
1622		1993
1623	/*****************************************************************************/	1994	/*****************************************************************************/
1624		1995
1625	#ifndef EV_HAVE_EV_TIME	1996	#ifndef EV_HAVE_EV_TIME
1626	ev_tstamp	1997	ev_tstamp
1627	ev_time (void) EV_THROW	1998	ev_time (void) EV_NOEXCEPT
1628	{	1999	{
1629	#if EV_USE_REALTIME	2000	#if EV_USE_REALTIME
1630	if (expect_true (have_realtime))	2001	if (ecb_expect_true (have_realtime))
1631	{	2002	{
1632	struct timespec ts;	2003	struct timespec ts;
1633	clock_gettime (CLOCK_REALTIME, &ts);	2004	clock_gettime (CLOCK_REALTIME, &ts);
1634	return ts.tv_sec + ts.tv_nsec * 1e-9;	2005	return EV_TS_GET (ts);
1635	}	2006	}
1636	#endif	2007	#endif
1637		2008
		2009	{
1638	struct timeval tv;	2010	struct timeval tv;
1639	gettimeofday (&tv, 0);	2011	gettimeofday (&tv, 0);
1640	return tv.tv_sec + tv.tv_usec * 1e-6;	2012	return EV_TV_GET (tv);
		2013	}
1641	}	2014	}
1642	#endif	2015	#endif
1643		2016
1644	inline_size ev_tstamp	2017	inline_size ev_tstamp
1645	get_clock (void)	2018	get_clock (void)
1646	{	2019	{
1647	#if EV_USE_MONOTONIC	2020	#if EV_USE_MONOTONIC
1648	if (expect_true (have_monotonic))	2021	if (ecb_expect_true (have_monotonic))
1649	{	2022	{
1650	struct timespec ts;	2023	struct timespec ts;
1651	clock_gettime (CLOCK_MONOTONIC, &ts);	2024	clock_gettime (CLOCK_MONOTONIC, &ts);
1652	return ts.tv_sec + ts.tv_nsec * 1e-9;	2025	return EV_TS_GET (ts);
1653	}	2026	}
1654	#endif	2027	#endif
1655		2028
1656	return ev_time ();	2029	return ev_time ();
1657	}	2030	}
1658		2031
1659	#if EV_MULTIPLICITY	2032	#if EV_MULTIPLICITY
1660	ev_tstamp	2033	ev_tstamp
1661	ev_now (EV_P) EV_THROW	2034	ev_now (EV_P) EV_NOEXCEPT
1662	{	2035	{
1663	return ev_rt_now;	2036	return ev_rt_now;
1664	}	2037	}
1665	#endif	2038	#endif
1666		2039
1667	void	2040	void
1668	ev_sleep (ev_tstamp delay) EV_THROW	2041	ev_sleep (ev_tstamp delay) EV_NOEXCEPT
1669	{	2042	{
1670	if (delay > 0.)	2043	if (delay > EV_TS_CONST (0.))
1671	{	2044	{
1672	#if EV_USE_NANOSLEEP	2045	#if EV_USE_NANOSLEEP
1673	struct timespec ts;	2046	struct timespec ts;
1674		2047
1675	EV_TS_SET (ts, delay);	2048	EV_TS_SET (ts, delay);
1676	nanosleep (&ts, 0);	2049	nanosleep (&ts, 0);
1677	#elif defined _WIN32	2050	#elif defined _WIN32
		2051	/* maybe this should round up, as ms is very low resolution */
		2052	/* compared to select (µs) or nanosleep (ns) */
1678	Sleep ((unsigned long)(delay * 1e3));	2053	Sleep ((unsigned long)(EV_TS_TO_MSEC (delay)));
1679	#else	2054	#else
1680	struct timeval tv;	2055	struct timeval tv;
1681		2056
1682	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */	2057	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */
1683	/* something not guaranteed by newer posix versions, but guaranteed */	2058	/* something not guaranteed by newer posix versions, but guaranteed */
…		…
1713	}	2088	}
1714		2089
1715	return ncur;	2090	return ncur;
1716	}	2091	}
1717		2092
1718	static void * noinline ecb_cold	2093	ecb_noinline ecb_cold
		2094	static void *
1719	array_realloc (int elem, void *base, int *cur, int cnt)	2095	array_realloc (int elem, void *base, int *cur, int cnt)
1720	{	2096	{
1721	*cur = array_nextsize (elem, *cur, cnt);	2097	*cur = array_nextsize (elem, *cur, cnt);
1722	return ev_realloc (base, elem * *cur);	2098	return ev_realloc (base, elem * *cur);
1723	}	2099	}
1724		2100
		2101	#define array_needsize_noinit(base,offset,count)
		2102
1725	#define array_init_zero(base,count) \	2103	#define array_needsize_zerofill(base,offset,count) \
1726	memset ((void *)(base), 0, sizeof (*(base)) * (count))	2104	memset ((void *)(base + offset), 0, sizeof (*(base)) * (count))
1727		2105
1728	#define array_needsize(type,base,cur,cnt,init) \	2106	#define array_needsize(type,base,cur,cnt,init) \
1729	if (expect_false ((cnt) > (cur))) \	2107	if (ecb_expect_false ((cnt) > (cur))) \
1730	{ \	2108	{ \
1731	int ecb_unused ocur_ = (cur); \	2109	ecb_unused int ocur_ = (cur); \
1732	(base) = (type *)array_realloc \	2110	(base) = (type *)array_realloc \
1733	(sizeof (type), (base), &(cur), (cnt)); \	2111	(sizeof (type), (base), &(cur), (cnt)); \
1734	init ((base) + (ocur_), (cur) - ocur_); \	2112	init ((base), ocur_, ((cur) - ocur_)); \
1735	}	2113	}
1736		2114
1737	#if 0	2115	#if 0
1738	#define array_slim(type,stem) \	2116	#define array_slim(type,stem) \
1739	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \	2117	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \
…		…
1748	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0	2126	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0
1749		2127
1750	/*****************************************************************************/	2128	/*****************************************************************************/
1751		2129
1752	/* dummy callback for pending events */	2130	/* dummy callback for pending events */
1753	static void noinline	2131	ecb_noinline
		2132	static void
1754	pendingcb (EV_P_ ev_prepare *w, int revents)	2133	pendingcb (EV_P_ ev_prepare *w, int revents)
1755	{	2134	{
1756	}	2135	}
1757		2136
1758	void noinline	2137	ecb_noinline
		2138	void
1759	ev_feed_event (EV_P_ void *w, int revents) EV_THROW	2139	ev_feed_event (EV_P_ void *w, int revents) EV_NOEXCEPT
1760	{	2140	{
1761	W w_ = (W)w;	2141	W w_ = (W)w;
1762	int pri = ABSPRI (w_);	2142	int pri = ABSPRI (w_);
1763		2143
1764	if (expect_false (w_->pending))	2144	if (ecb_expect_false (w_->pending))
1765	pendings [pri][w_->pending - 1].events |= revents;	2145	pendings [pri][w_->pending - 1].events |= revents;
1766	else	2146	else
1767	{	2147	{
1768	w_->pending = ++pendingcnt [pri];	2148	w_->pending = ++pendingcnt [pri];
1769	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, EMPTY2);	2149	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, array_needsize_noinit);
1770	pendings [pri][w_->pending - 1].w = w_;	2150	pendings [pri][w_->pending - 1].w = w_;
1771	pendings [pri][w_->pending - 1].events = revents;	2151	pendings [pri][w_->pending - 1].events = revents;
1772	}	2152	}
1773		2153
1774	pendingpri = NUMPRI - 1;	2154	pendingpri = NUMPRI - 1;
1775	}	2155	}
1776		2156
1777	inline_speed void	2157	inline_speed void
1778	feed_reverse (EV_P_ W w)	2158	feed_reverse (EV_P_ W w)
1779	{	2159	{
1780	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, EMPTY2);	2160	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, array_needsize_noinit);
1781	rfeeds [rfeedcnt++] = w;	2161	rfeeds [rfeedcnt++] = w;
1782	}	2162	}
1783		2163
1784	inline_size void	2164	inline_size void
1785	feed_reverse_done (EV_P_ int revents)	2165	feed_reverse_done (EV_P_ int revents)
…		…
1820	inline_speed void	2200	inline_speed void
1821	fd_event (EV_P_ int fd, int revents)	2201	fd_event (EV_P_ int fd, int revents)
1822	{	2202	{
1823	ANFD *anfd = anfds + fd;	2203	ANFD *anfd = anfds + fd;
1824		2204
1825	if (expect_true (!anfd->reify))	2205	if (ecb_expect_true (!anfd->reify))
1826	fd_event_nocheck (EV_A_ fd, revents);	2206	fd_event_nocheck (EV_A_ fd, revents);
1827	}	2207	}
1828		2208
1829	void	2209	void
1830	ev_feed_fd_event (EV_P_ int fd, int revents) EV_THROW	2210	ev_feed_fd_event (EV_P_ int fd, int revents) EV_NOEXCEPT
1831	{	2211	{
1832	if (fd >= 0 && fd < anfdmax)	2212	if (fd >= 0 && fd < anfdmax)
1833	fd_event_nocheck (EV_A_ fd, revents);	2213	fd_event_nocheck (EV_A_ fd, revents);
1834	}	2214	}
1835		2215
…		…
1872	ev_io *w;	2252	ev_io *w;
1873		2253
1874	unsigned char o_events = anfd->events;	2254	unsigned char o_events = anfd->events;
1875	unsigned char o_reify = anfd->reify;	2255	unsigned char o_reify = anfd->reify;
1876		2256
1877	anfd->reify = 0;	2257	anfd->reify = 0;
1878		2258
1879	/*if (expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */	2259	/*if (ecb_expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */
1880	{	2260	{
1881	anfd->events = 0;	2261	anfd->events = 0;
1882		2262
1883	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)	2263	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)
1884	anfd->events |= (unsigned char)w->events;	2264	anfd->events |= (unsigned char)w->events;
…		…
1893		2273
1894	fdchangecnt = 0;	2274	fdchangecnt = 0;
1895	}	2275	}
1896		2276
1897	/* something about the given fd changed */	2277	/* something about the given fd changed */
1898	inline_size void	2278	inline_size
		2279	void
1899	fd_change (EV_P_ int fd, int flags)	2280	fd_change (EV_P_ int fd, int flags)
1900	{	2281	{
1901	unsigned char reify = anfds [fd].reify;	2282	unsigned char reify = anfds [fd].reify;
1902	anfds [fd].reify |= flags;	2283	anfds [fd].reify |= flags;
1903		2284
1904	if (expect_true (!reify))	2285	if (ecb_expect_true (!reify))
1905	{	2286	{
1906	++fdchangecnt;	2287	++fdchangecnt;
1907	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, EMPTY2);	2288	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, array_needsize_noinit);
1908	fdchanges [fdchangecnt - 1] = fd;	2289	fdchanges [fdchangecnt - 1] = fd;
1909	}	2290	}
1910	}	2291	}
1911		2292
1912	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */	2293	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */
1913	inline_speed void ecb_cold	2294	inline_speed ecb_cold void
1914	fd_kill (EV_P_ int fd)	2295	fd_kill (EV_P_ int fd)
1915	{	2296	{
1916	ev_io *w;	2297	ev_io *w;
1917		2298
1918	while ((w = (ev_io *)anfds [fd].head))	2299	while ((w = (ev_io *)anfds [fd].head))
…		…
1921	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);	2302	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);
1922	}	2303	}
1923	}	2304	}
1924		2305
1925	/* check whether the given fd is actually valid, for error recovery */	2306	/* check whether the given fd is actually valid, for error recovery */
1926	inline_size int ecb_cold	2307	inline_size ecb_cold int
1927	fd_valid (int fd)	2308	fd_valid (int fd)
1928	{	2309	{
1929	#ifdef _WIN32	2310	#ifdef _WIN32
1930	return EV_FD_TO_WIN32_HANDLE (fd) != -1;	2311	return EV_FD_TO_WIN32_HANDLE (fd) != -1;
1931	#else	2312	#else
1932	return fcntl (fd, F_GETFD) != -1;	2313	return fcntl (fd, F_GETFD) != -1;
1933	#endif	2314	#endif
1934	}	2315	}
1935		2316
1936	/* called on EBADF to verify fds */	2317	/* called on EBADF to verify fds */
1937	static void noinline ecb_cold	2318	ecb_noinline ecb_cold
		2319	static void
1938	fd_ebadf (EV_P)	2320	fd_ebadf (EV_P)
1939	{	2321	{
1940	int fd;	2322	int fd;
1941		2323
1942	for (fd = 0; fd < anfdmax; ++fd)	2324	for (fd = 0; fd < anfdmax; ++fd)
…		…
1944	if (!fd_valid (fd) && errno == EBADF)	2326	if (!fd_valid (fd) && errno == EBADF)
1945	fd_kill (EV_A_ fd);	2327	fd_kill (EV_A_ fd);
1946	}	2328	}
1947		2329
1948	/* called on ENOMEM in select/poll to kill some fds and retry */	2330	/* called on ENOMEM in select/poll to kill some fds and retry */
1949	static void noinline ecb_cold	2331	ecb_noinline ecb_cold
		2332	static void
1950	fd_enomem (EV_P)	2333	fd_enomem (EV_P)
1951	{	2334	{
1952	int fd;	2335	int fd;
1953		2336
1954	for (fd = anfdmax; fd--; )	2337	for (fd = anfdmax; fd--; )
…		…
1958	break;	2341	break;
1959	}	2342	}
1960	}	2343	}
1961		2344
1962	/* usually called after fork if backend needs to re-arm all fds from scratch */	2345	/* usually called after fork if backend needs to re-arm all fds from scratch */
1963	static void noinline	2346	ecb_noinline
		2347	static void
1964	fd_rearm_all (EV_P)	2348	fd_rearm_all (EV_P)
1965	{	2349	{
1966	int fd;	2350	int fd;
1967		2351
1968	for (fd = 0; fd < anfdmax; ++fd)	2352	for (fd = 0; fd < anfdmax; ++fd)
…		…
2021	ev_tstamp minat;	2405	ev_tstamp minat;
2022	ANHE *minpos;	2406	ANHE *minpos;
2023	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;	2407	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;
2024		2408
2025	/* find minimum child */	2409	/* find minimum child */
2026	if (expect_true (pos + DHEAP - 1 < E))	2410	if (ecb_expect_true (pos + DHEAP - 1 < E))
2027	{	2411	{
2028	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));	2412	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));
2029	if ( ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));	2413	if ( minat > ANHE_at (pos [1])) (minpos = pos + 1), (minat = ANHE_at (*minpos));
2030	if ( ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));	2414	if ( minat > ANHE_at (pos [2])) (minpos = pos + 2), (minat = ANHE_at (*minpos));
2031	if ( ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));	2415	if ( minat > ANHE_at (pos [3])) (minpos = pos + 3), (minat = ANHE_at (*minpos));
2032	}	2416	}
2033	else if (pos < E)	2417	else if (pos < E)
2034	{	2418	{
2035	/* slow path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));	2419	/* slow path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));
2036	if (pos + 1 < E && ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));	2420	if (pos + 1 < E && minat > ANHE_at (pos [1])) (minpos = pos + 1), (minat = ANHE_at (*minpos));
2037	if (pos + 2 < E && ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));	2421	if (pos + 2 < E && minat > ANHE_at (pos [2])) (minpos = pos + 2), (minat = ANHE_at (*minpos));
2038	if (pos + 3 < E && ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));	2422	if (pos + 3 < E && minat > ANHE_at (pos [3])) (minpos = pos + 3), (minat = ANHE_at (*minpos));
2039	}	2423	}
2040	else	2424	else
2041	break;	2425	break;
2042		2426
2043	if (ANHE_at (he) <= minat)	2427	if (ANHE_at (he) <= minat)
…		…
2051		2435
2052	heap [k] = he;	2436	heap [k] = he;
2053	ev_active (ANHE_w (he)) = k;	2437	ev_active (ANHE_w (he)) = k;
2054	}	2438	}
2055		2439
2056	#else /* 4HEAP */	2440	#else /* not 4HEAP */
2057		2441
2058	#define HEAP0 1	2442	#define HEAP0 1
2059	#define HPARENT(k) ((k) >> 1)	2443	#define HPARENT(k) ((k) >> 1)
2060	#define UPHEAP_DONE(p,k) (!(p))	2444	#define UPHEAP_DONE(p,k) (!(p))
2061		2445
…		…
2149		2533
2150	/*****************************************************************************/	2534	/*****************************************************************************/
2151		2535
2152	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	2536	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2153		2537
2154	static void noinline ecb_cold	2538	ecb_noinline ecb_cold
		2539	static void
2155	evpipe_init (EV_P)	2540	evpipe_init (EV_P)
2156	{	2541	{
2157	if (!ev_is_active (&pipe_w))	2542	if (!ev_is_active (&pipe_w))
2158	{	2543	{
2159	int fds [2];	2544	int fds [2];
…		…
2199	inline_speed void	2584	inline_speed void
2200	evpipe_write (EV_P_ EV_ATOMIC_T *flag)	2585	evpipe_write (EV_P_ EV_ATOMIC_T *flag)
2201	{	2586	{
2202	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */	2587	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */
2203		2588
2204	if (expect_true (*flag))	2589	if (ecb_expect_true (*flag))
2205	return;	2590	return;
2206		2591
2207	*flag = 1;	2592	*flag = 1;
2208	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */	2593	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */
2209		2594
…		…
2230	#endif	2615	#endif
2231	{	2616	{
2232	#ifdef _WIN32	2617	#ifdef _WIN32
2233	WSABUF buf;	2618	WSABUF buf;
2234	DWORD sent;	2619	DWORD sent;
2235	buf.buf = &buf;	2620	buf.buf = (char *)&buf;
2236	buf.len = 1;	2621	buf.len = 1;
2237	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);	2622	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);
2238	#else	2623	#else
2239	write (evpipe [1], &(evpipe [1]), 1);	2624	write (evpipe [1], &(evpipe [1]), 1);
2240	#endif	2625	#endif
…		…
2286	sig_pending = 0;	2671	sig_pending = 0;
2287		2672
2288	ECB_MEMORY_FENCE;	2673	ECB_MEMORY_FENCE;
2289		2674
2290	for (i = EV_NSIG - 1; i--; )	2675	for (i = EV_NSIG - 1; i--; )
2291	if (expect_false (signals [i].pending))	2676	if (ecb_expect_false (signals [i].pending))
2292	ev_feed_signal_event (EV_A_ i + 1);	2677	ev_feed_signal_event (EV_A_ i + 1);
2293	}	2678	}
2294	#endif	2679	#endif
2295		2680
2296	#if EV_ASYNC_ENABLE	2681	#if EV_ASYNC_ENABLE
…		…
2312	}	2697	}
2313		2698
2314	/*****************************************************************************/	2699	/*****************************************************************************/
2315		2700
2316	void	2701	void
2317	ev_feed_signal (int signum) EV_THROW	2702	ev_feed_signal (int signum) EV_NOEXCEPT
2318	{	2703	{
2319	#if EV_MULTIPLICITY	2704	#if EV_MULTIPLICITY
2320	EV_P;	2705	EV_P;
2321	ECB_MEMORY_FENCE_ACQUIRE;	2706	ECB_MEMORY_FENCE_ACQUIRE;
2322	EV_A = signals [signum - 1].loop;	2707	EV_A = signals [signum - 1].loop;
…		…
2337	#endif	2722	#endif
2338		2723
2339	ev_feed_signal (signum);	2724	ev_feed_signal (signum);
2340	}	2725	}
2341		2726
2342	void noinline	2727	ecb_noinline
		2728	void
2343	ev_feed_signal_event (EV_P_ int signum) EV_THROW	2729	ev_feed_signal_event (EV_P_ int signum) EV_NOEXCEPT
2344	{	2730	{
2345	WL w;	2731	WL w;
2346		2732
2347	if (expect_false (signum <= 0 || signum >= EV_NSIG))	2733	if (ecb_expect_false (signum <= 0 || signum >= EV_NSIG))
2348	return;	2734	return;
2349		2735
2350	--signum;	2736	--signum;
2351		2737
2352	#if EV_MULTIPLICITY	2738	#if EV_MULTIPLICITY
2353	/* it is permissible to try to feed a signal to the wrong loop */	2739	/* it is permissible to try to feed a signal to the wrong loop */
2354	/* or, likely more useful, feeding a signal nobody is waiting for */	2740	/* or, likely more useful, feeding a signal nobody is waiting for */
2355		2741
2356	if (expect_false (signals [signum].loop != EV_A))	2742	if (ecb_expect_false (signals [signum].loop != EV_A))
2357	return;	2743	return;
2358	#endif	2744	#endif
2359		2745
2360	signals [signum].pending = 0;	2746	signals [signum].pending = 0;
2361	ECB_MEMORY_FENCE_RELEASE;	2747	ECB_MEMORY_FENCE_RELEASE;
…		…
2457	# include "ev_kqueue.c"	2843	# include "ev_kqueue.c"
2458	#endif	2844	#endif
2459	#if EV_USE_EPOLL	2845	#if EV_USE_EPOLL
2460	# include "ev_epoll.c"	2846	# include "ev_epoll.c"
2461	#endif	2847	#endif
		2848	#if EV_USE_LINUXAIO
		2849	# include "ev_linuxaio.c"
		2850	#endif
		2851	#if EV_USE_IOURING
		2852	# include "ev_iouring.c"
		2853	#endif
2462	#if EV_USE_POLL	2854	#if EV_USE_POLL
2463	# include "ev_poll.c"	2855	# include "ev_poll.c"
2464	#endif	2856	#endif
2465	#if EV_USE_SELECT	2857	#if EV_USE_SELECT
2466	# include "ev_select.c"	2858	# include "ev_select.c"
2467	#endif	2859	#endif
2468		2860
2469	int ecb_cold	2861	ecb_cold int
2470	ev_version_major (void) EV_THROW	2862	ev_version_major (void) EV_NOEXCEPT
2471	{	2863	{
2472	return EV_VERSION_MAJOR;	2864	return EV_VERSION_MAJOR;
2473	}	2865	}
2474		2866
2475	int ecb_cold	2867	ecb_cold int
2476	ev_version_minor (void) EV_THROW	2868	ev_version_minor (void) EV_NOEXCEPT
2477	{	2869	{
2478	return EV_VERSION_MINOR;	2870	return EV_VERSION_MINOR;
2479	}	2871	}
2480		2872
2481	/* return true if we are running with elevated privileges and should ignore env variables */	2873	/* return true if we are running with elevated privileges and should ignore env variables */
2482	int inline_size ecb_cold	2874	inline_size ecb_cold int
2483	enable_secure (void)	2875	enable_secure (void)
2484	{	2876	{
2485	#ifdef _WIN32	2877	#ifdef _WIN32
2486	return 0;	2878	return 0;
2487	#else	2879	#else
2488	return getuid () != geteuid ()	2880	return getuid () != geteuid ()
2489	|| getgid () != getegid ();	2881	|| getgid () != getegid ();
2490	#endif	2882	#endif
2491	}	2883	}
2492		2884
2493	unsigned int ecb_cold	2885	ecb_cold
		2886	unsigned int
2494	ev_supported_backends (void) EV_THROW	2887	ev_supported_backends (void) EV_NOEXCEPT
2495	{	2888	{
2496	unsigned int flags = 0;	2889	unsigned int flags = 0;
2497		2890
2498	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;	2891	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;
2499	if (EV_USE_KQUEUE) flags |= EVBACKEND_KQUEUE;	2892	if (EV_USE_KQUEUE ) flags |= EVBACKEND_KQUEUE;
2500	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;	2893	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;
		2894	if (EV_USE_LINUXAIO) flags |= EVBACKEND_LINUXAIO;
		2895	if (EV_USE_IOURING ) flags |= EVBACKEND_IOURING;
2501	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;	2896	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;
2502	if (EV_USE_SELECT) flags |= EVBACKEND_SELECT;	2897	if (EV_USE_SELECT ) flags |= EVBACKEND_SELECT;
2503		2898
2504	return flags;	2899	return flags;
2505	}	2900	}
2506		2901
2507	unsigned int ecb_cold	2902	ecb_cold
		2903	unsigned int
2508	ev_recommended_backends (void) EV_THROW	2904	ev_recommended_backends (void) EV_NOEXCEPT
2509	{	2905	{
2510	unsigned int flags = ev_supported_backends ();	2906	unsigned int flags = ev_supported_backends ();
2511		2907
2512	#ifndef __NetBSD__	2908	#ifndef __NetBSD__
2513	/* kqueue is borked on everything but netbsd apparently */	2909	/* kqueue is borked on everything but netbsd apparently */
…		…
2521	#endif	2917	#endif
2522	#ifdef __FreeBSD__	2918	#ifdef __FreeBSD__
2523	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */	2919	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */
2524	#endif	2920	#endif
2525		2921
		2922	/* TODO: linuxaio is very experimental */
		2923	#if !EV_RECOMMEND_LINUXAIO
		2924	flags &= ~EVBACKEND_LINUXAIO;
		2925	#endif
		2926	/* TODO: linuxaio is super experimental */
		2927	#if !EV_RECOMMEND_IOURING
		2928	flags &= ~EVBACKEND_IOURING;
		2929	#endif
		2930
2526	return flags;	2931	return flags;
2527	}	2932	}
2528		2933
2529	unsigned int ecb_cold	2934	ecb_cold
		2935	unsigned int
2530	ev_embeddable_backends (void) EV_THROW	2936	ev_embeddable_backends (void) EV_NOEXCEPT
2531	{	2937	{
2532	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;	2938	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;
2533		2939
2534	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */	2940	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */
2535	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */	2941	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */
2536	flags &= ~EVBACKEND_EPOLL;	2942	flags &= ~EVBACKEND_EPOLL;
2537		2943
		2944	/* EVBACKEND_LINUXAIO is theoretically embeddable, but suffers from a performance overhead */
		2945
		2946	/* EVBACKEND_IOURING is practically embeddable, but the current implementation is not
		2947	* because our backend_fd is the epoll fd we need as fallback.
		2948	* if the kernel ever is fixed, this might change...
		2949	*/
		2950
2538	return flags;	2951	return flags;
2539	}	2952	}
2540		2953
2541	unsigned int	2954	unsigned int
2542	ev_backend (EV_P) EV_THROW	2955	ev_backend (EV_P) EV_NOEXCEPT
2543	{	2956	{
2544	return backend;	2957	return backend;
2545	}	2958	}
2546		2959
2547	#if EV_FEATURE_API	2960	#if EV_FEATURE_API
2548	unsigned int	2961	unsigned int
2549	ev_iteration (EV_P) EV_THROW	2962	ev_iteration (EV_P) EV_NOEXCEPT
2550	{	2963	{
2551	return loop_count;	2964	return loop_count;
2552	}	2965	}
2553		2966
2554	unsigned int	2967	unsigned int
2555	ev_depth (EV_P) EV_THROW	2968	ev_depth (EV_P) EV_NOEXCEPT
2556	{	2969	{
2557	return loop_depth;	2970	return loop_depth;
2558	}	2971	}
2559		2972
2560	void	2973	void
2561	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2974	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2562	{	2975	{
2563	io_blocktime = interval;	2976	io_blocktime = interval;
2564	}	2977	}
2565		2978
2566	void	2979	void
2567	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2980	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2568	{	2981	{
2569	timeout_blocktime = interval;	2982	timeout_blocktime = interval;
2570	}	2983	}
2571		2984
2572	void	2985	void
2573	ev_set_userdata (EV_P_ void *data) EV_THROW	2986	ev_set_userdata (EV_P_ void *data) EV_NOEXCEPT
2574	{	2987	{
2575	userdata = data;	2988	userdata = data;
2576	}	2989	}
2577		2990
2578	void *	2991	void *
2579	ev_userdata (EV_P) EV_THROW	2992	ev_userdata (EV_P) EV_NOEXCEPT
2580	{	2993	{
2581	return userdata;	2994	return userdata;
2582	}	2995	}
2583		2996
2584	void	2997	void
2585	ev_set_invoke_pending_cb (EV_P_ ev_loop_callback invoke_pending_cb) EV_THROW	2998	ev_set_invoke_pending_cb (EV_P_ ev_loop_callback invoke_pending_cb) EV_NOEXCEPT
2586	{	2999	{
2587	invoke_cb = invoke_pending_cb;	3000	invoke_cb = invoke_pending_cb;
2588	}	3001	}
2589		3002
2590	void	3003	void
2591	ev_set_loop_release_cb (EV_P_ ev_loop_callback_nothrow release, ev_loop_callback_nothrow acquire) EV_THROW	3004	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_NOEXCEPT, void (*acquire)(EV_P) EV_NOEXCEPT) EV_NOEXCEPT
2592	{	3005	{
2593	release_cb = release;	3006	release_cb = release;
2594	acquire_cb = acquire;	3007	acquire_cb = acquire;
2595	}	3008	}
2596	#endif	3009	#endif
2597		3010
2598	/* initialise a loop structure, must be zero-initialised */	3011	/* initialise a loop structure, must be zero-initialised */
2599	static void noinline ecb_cold	3012	ecb_noinline ecb_cold
		3013	static void
2600	loop_init (EV_P_ unsigned int flags) EV_THROW	3014	loop_init (EV_P_ unsigned int flags) EV_NOEXCEPT
2601	{	3015	{
2602	if (!backend)	3016	if (!backend)
2603	{	3017	{
2604	origflags = flags;	3018	origflags = flags;
2605		3019
…		…
2663		3077
2664	if (!(flags & EVBACKEND_MASK))	3078	if (!(flags & EVBACKEND_MASK))
2665	flags |= ev_recommended_backends ();	3079	flags |= ev_recommended_backends ();
2666		3080
2667	#if EV_USE_IOCP	3081	#if EV_USE_IOCP
2668	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);	3082	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);
2669	#endif	3083	#endif
2670	#if EV_USE_PORT	3084	#if EV_USE_PORT
2671	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);	3085	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);
2672	#endif	3086	#endif
2673	#if EV_USE_KQUEUE	3087	#if EV_USE_KQUEUE
2674	if (!backend && (flags & EVBACKEND_KQUEUE)) backend = kqueue_init (EV_A_ flags);	3088	if (!backend && (flags & EVBACKEND_KQUEUE )) backend = kqueue_init (EV_A_ flags);
		3089	#endif
		3090	#if EV_USE_IOURING
		3091	if (!backend && (flags & EVBACKEND_IOURING )) backend = iouring_init (EV_A_ flags);
		3092	#endif
		3093	#if EV_USE_LINUXAIO
		3094	if (!backend && (flags & EVBACKEND_LINUXAIO)) backend = linuxaio_init (EV_A_ flags);
2675	#endif	3095	#endif
2676	#if EV_USE_EPOLL	3096	#if EV_USE_EPOLL
2677	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);	3097	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);
2678	#endif	3098	#endif
2679	#if EV_USE_POLL	3099	#if EV_USE_POLL
2680	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);	3100	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);
2681	#endif	3101	#endif
2682	#if EV_USE_SELECT	3102	#if EV_USE_SELECT
2683	if (!backend && (flags & EVBACKEND_SELECT)) backend = select_init (EV_A_ flags);	3103	if (!backend && (flags & EVBACKEND_SELECT )) backend = select_init (EV_A_ flags);
2684	#endif	3104	#endif
2685		3105
2686	ev_prepare_init (&pending_w, pendingcb);	3106	ev_prepare_init (&pending_w, pendingcb);
2687		3107
2688	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	3108	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
…		…
2691	#endif	3111	#endif
2692	}	3112	}
2693	}	3113	}
2694		3114
2695	/* free up a loop structure */	3115	/* free up a loop structure */
2696	void ecb_cold	3116	ecb_cold
		3117	void
2697	ev_loop_destroy (EV_P)	3118	ev_loop_destroy (EV_P)
2698	{	3119	{
2699	int i;	3120	int i;
2700		3121
2701	#if EV_MULTIPLICITY	3122	#if EV_MULTIPLICITY
…		…
2704	return;	3125	return;
2705	#endif	3126	#endif
2706		3127
2707	#if EV_CLEANUP_ENABLE	3128	#if EV_CLEANUP_ENABLE
2708	/* queue cleanup watchers (and execute them) */	3129	/* queue cleanup watchers (and execute them) */
2709	if (expect_false (cleanupcnt))	3130	if (ecb_expect_false (cleanupcnt))
2710	{	3131	{
2711	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);	3132	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);
2712	EV_INVOKE_PENDING;	3133	EV_INVOKE_PENDING;
2713	}	3134	}
2714	#endif	3135	#endif
…		…
2742		3163
2743	if (backend_fd >= 0)	3164	if (backend_fd >= 0)
2744	close (backend_fd);	3165	close (backend_fd);
2745		3166
2746	#if EV_USE_IOCP	3167	#if EV_USE_IOCP
2747	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);	3168	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);
2748	#endif	3169	#endif
2749	#if EV_USE_PORT	3170	#if EV_USE_PORT
2750	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);	3171	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);
2751	#endif	3172	#endif
2752	#if EV_USE_KQUEUE	3173	#if EV_USE_KQUEUE
2753	if (backend == EVBACKEND_KQUEUE) kqueue_destroy (EV_A);	3174	if (backend == EVBACKEND_KQUEUE ) kqueue_destroy (EV_A);
		3175	#endif
		3176	#if EV_USE_IOURING
		3177	if (backend == EVBACKEND_IOURING ) iouring_destroy (EV_A);
		3178	#endif
		3179	#if EV_USE_LINUXAIO
		3180	if (backend == EVBACKEND_LINUXAIO) linuxaio_destroy (EV_A);
2754	#endif	3181	#endif
2755	#if EV_USE_EPOLL	3182	#if EV_USE_EPOLL
2756	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);	3183	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);
2757	#endif	3184	#endif
2758	#if EV_USE_POLL	3185	#if EV_USE_POLL
2759	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);	3186	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);
2760	#endif	3187	#endif
2761	#if EV_USE_SELECT	3188	#if EV_USE_SELECT
2762	if (backend == EVBACKEND_SELECT) select_destroy (EV_A);	3189	if (backend == EVBACKEND_SELECT ) select_destroy (EV_A);
2763	#endif	3190	#endif
2764		3191
2765	for (i = NUMPRI; i--; )	3192	for (i = NUMPRI; i--; )
2766	{	3193	{
2767	array_free (pending, [i]);	3194	array_free (pending, [i]);
…		…
2809		3236
2810	inline_size void	3237	inline_size void
2811	loop_fork (EV_P)	3238	loop_fork (EV_P)
2812	{	3239	{
2813	#if EV_USE_PORT	3240	#if EV_USE_PORT
2814	if (backend == EVBACKEND_PORT ) port_fork (EV_A);	3241	if (backend == EVBACKEND_PORT ) port_fork (EV_A);
2815	#endif	3242	#endif
2816	#if EV_USE_KQUEUE	3243	#if EV_USE_KQUEUE
2817	if (backend == EVBACKEND_KQUEUE) kqueue_fork (EV_A);	3244	if (backend == EVBACKEND_KQUEUE ) kqueue_fork (EV_A);
		3245	#endif
		3246	#if EV_USE_IOURING
		3247	if (backend == EVBACKEND_IOURING ) iouring_fork (EV_A);
		3248	#endif
		3249	#if EV_USE_LINUXAIO
		3250	if (backend == EVBACKEND_LINUXAIO) linuxaio_fork (EV_A);
2818	#endif	3251	#endif
2819	#if EV_USE_EPOLL	3252	#if EV_USE_EPOLL
2820	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);	3253	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);
2821	#endif	3254	#endif
2822	#if EV_USE_INOTIFY	3255	#if EV_USE_INOTIFY
2823	infy_fork (EV_A);	3256	infy_fork (EV_A);
2824	#endif	3257	#endif
2825		3258
2826	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	3259	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2827	if (ev_is_active (&pipe_w))	3260	if (ev_is_active (&pipe_w) && postfork != 2)
2828	{	3261	{
2829	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */	3262	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */
2830		3263
2831	ev_ref (EV_A);	3264	ev_ref (EV_A);
2832	ev_io_stop (EV_A_ &pipe_w);	3265	ev_io_stop (EV_A_ &pipe_w);
…		…
2843	postfork = 0;	3276	postfork = 0;
2844	}	3277	}
2845		3278
2846	#if EV_MULTIPLICITY	3279	#if EV_MULTIPLICITY
2847		3280
		3281	ecb_cold
2848	struct ev_loop * ecb_cold	3282	struct ev_loop *
2849	ev_loop_new (unsigned int flags) EV_THROW	3283	ev_loop_new (unsigned int flags) EV_NOEXCEPT
2850	{	3284	{
2851	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));	3285	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));
2852		3286
2853	memset (EV_A, 0, sizeof (struct ev_loop));	3287	memset (EV_A, 0, sizeof (struct ev_loop));
2854	loop_init (EV_A_ flags);	3288	loop_init (EV_A_ flags);
…		…
2861	}	3295	}
2862		3296
2863	#endif /* multiplicity */	3297	#endif /* multiplicity */
2864		3298
2865	#if EV_VERIFY	3299	#if EV_VERIFY
2866	static void noinline ecb_cold	3300	ecb_noinline ecb_cold
		3301	static void
2867	verify_watcher (EV_P_ W w)	3302	verify_watcher (EV_P_ W w)
2868	{	3303	{
2869	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));	3304	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));
2870		3305
2871	if (w->pending)	3306	if (w->pending)
2872	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));	3307	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));
2873	}	3308	}
2874		3309
2875	static void noinline ecb_cold	3310	ecb_noinline ecb_cold
		3311	static void
2876	verify_heap (EV_P_ ANHE *heap, int N)	3312	verify_heap (EV_P_ ANHE *heap, int N)
2877	{	3313	{
2878	int i;	3314	int i;
2879		3315
2880	for (i = HEAP0; i < N + HEAP0; ++i)	3316	for (i = HEAP0; i < N + HEAP0; ++i)
…		…
2885		3321
2886	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));	3322	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));
2887	}	3323	}
2888	}	3324	}
2889		3325
2890	static void noinline ecb_cold	3326	ecb_noinline ecb_cold
		3327	static void
2891	array_verify (EV_P_ W *ws, int cnt)	3328	array_verify (EV_P_ W *ws, int cnt)
2892	{	3329	{
2893	while (cnt--)	3330	while (cnt--)
2894	{	3331	{
2895	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));	3332	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));
…		…
2898	}	3335	}
2899	#endif	3336	#endif
2900		3337
2901	#if EV_FEATURE_API	3338	#if EV_FEATURE_API
2902	void ecb_cold	3339	void ecb_cold
2903	ev_verify (EV_P) EV_THROW	3340	ev_verify (EV_P) EV_NOEXCEPT
2904	{	3341	{
2905	#if EV_VERIFY	3342	#if EV_VERIFY
2906	int i;	3343	int i;
2907	WL w, w2;	3344	WL w, w2;
2908		3345
…		…
2984	#endif	3421	#endif
2985	}	3422	}
2986	#endif	3423	#endif
2987		3424
2988	#if EV_MULTIPLICITY	3425	#if EV_MULTIPLICITY
		3426	ecb_cold
2989	struct ev_loop * ecb_cold	3427	struct ev_loop *
2990	#else	3428	#else
2991	int	3429	int
2992	#endif	3430	#endif
2993	ev_default_loop (unsigned int flags) EV_THROW	3431	ev_default_loop (unsigned int flags) EV_NOEXCEPT
2994	{	3432	{
2995	if (!ev_default_loop_ptr)	3433	if (!ev_default_loop_ptr)
2996	{	3434	{
2997	#if EV_MULTIPLICITY	3435	#if EV_MULTIPLICITY
2998	EV_P = ev_default_loop_ptr = &default_loop_struct;	3436	EV_P = ev_default_loop_ptr = &default_loop_struct;
…		…
3017		3455
3018	return ev_default_loop_ptr;	3456	return ev_default_loop_ptr;
3019	}	3457	}
3020		3458
3021	void	3459	void
3022	ev_loop_fork (EV_P) EV_THROW	3460	ev_loop_fork (EV_P) EV_NOEXCEPT
3023	{	3461	{
3024	postfork = 1;	3462	postfork = 1;
3025	}	3463	}
3026		3464
3027	/*****************************************************************************/	3465	/*****************************************************************************/
…		…
3031	{	3469	{
3032	EV_CB_INVOKE ((W)w, revents);	3470	EV_CB_INVOKE ((W)w, revents);
3033	}	3471	}
3034		3472
3035	unsigned int	3473	unsigned int
3036	ev_pending_count (EV_P) EV_THROW	3474	ev_pending_count (EV_P) EV_NOEXCEPT
3037	{	3475	{
3038	int pri;	3476	int pri;
3039	unsigned int count = 0;	3477	unsigned int count = 0;
3040		3478
3041	for (pri = NUMPRI; pri--; )	3479	for (pri = NUMPRI; pri--; )
3042	count += pendingcnt [pri];	3480	count += pendingcnt [pri];
3043		3481
3044	return count;	3482	return count;
3045	}	3483	}
3046		3484
3047	void noinline	3485	ecb_noinline
		3486	void
3048	ev_invoke_pending (EV_P)	3487	ev_invoke_pending (EV_P)
3049	{	3488	{
3050	pendingpri = NUMPRI;	3489	pendingpri = NUMPRI;
3051		3490
3052	while (pendingpri) /* pendingpri possibly gets modified in the inner loop */	3491	do
3053	{	3492	{
3054	--pendingpri;	3493	--pendingpri;
3055		3494
		3495	/* pendingpri possibly gets modified in the inner loop */
3056	while (pendingcnt [pendingpri])	3496	while (pendingcnt [pendingpri])
3057	{	3497	{
3058	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];	3498	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];
3059		3499
3060	p->w->pending = 0;	3500	p->w->pending = 0;
3061	EV_CB_INVOKE (p->w, p->events);	3501	EV_CB_INVOKE (p->w, p->events);
3062	EV_FREQUENT_CHECK;	3502	EV_FREQUENT_CHECK;
3063	}	3503	}
3064	}	3504	}
		3505	while (pendingpri);
3065	}	3506	}
3066		3507
3067	#if EV_IDLE_ENABLE	3508	#if EV_IDLE_ENABLE
3068	/* make idle watchers pending. this handles the "call-idle */	3509	/* make idle watchers pending. this handles the "call-idle */
3069	/* only when higher priorities are idle" logic */	3510	/* only when higher priorities are idle" logic */
3070	inline_size void	3511	inline_size void
3071	idle_reify (EV_P)	3512	idle_reify (EV_P)
3072	{	3513	{
3073	if (expect_false (idleall))	3514	if (ecb_expect_false (idleall))
3074	{	3515	{
3075	int pri;	3516	int pri;
3076		3517
3077	for (pri = NUMPRI; pri--; )	3518	for (pri = NUMPRI; pri--; )
3078	{	3519	{
…		…
3108	{	3549	{
3109	ev_at (w) += w->repeat;	3550	ev_at (w) += w->repeat;
3110	if (ev_at (w) < mn_now)	3551	if (ev_at (w) < mn_now)
3111	ev_at (w) = mn_now;	3552	ev_at (w) = mn_now;
3112		3553
3113	assert (("libev: negative ev_timer repeat value found while processing timers", w->repeat > 0.));	3554	assert (("libev: negative ev_timer repeat value found while processing timers", w->repeat > EV_TS_CONST (0.)));
3114		3555
3115	ANHE_at_cache (timers [HEAP0]);	3556	ANHE_at_cache (timers [HEAP0]);
3116	downheap (timers, timercnt, HEAP0);	3557	downheap (timers, timercnt, HEAP0);
3117	}	3558	}
3118	else	3559	else
…		…
3127	}	3568	}
3128	}	3569	}
3129		3570
3130	#if EV_PERIODIC_ENABLE	3571	#if EV_PERIODIC_ENABLE
3131		3572
3132	static void noinline	3573	ecb_noinline
		3574	static void
3133	periodic_recalc (EV_P_ ev_periodic *w)	3575	periodic_recalc (EV_P_ ev_periodic *w)
3134	{	3576	{
3135	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;	3577	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;
3136	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);	3578	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);
3137		3579
…		…
3139	while (at <= ev_rt_now)	3581	while (at <= ev_rt_now)
3140	{	3582	{
3141	ev_tstamp nat = at + w->interval;	3583	ev_tstamp nat = at + w->interval;
3142		3584
3143	/* when resolution fails us, we use ev_rt_now */	3585	/* when resolution fails us, we use ev_rt_now */
3144	if (expect_false (nat == at))	3586	if (ecb_expect_false (nat == at))
3145	{	3587	{
3146	at = ev_rt_now;	3588	at = ev_rt_now;
3147	break;	3589	break;
3148	}	3590	}
3149		3591
…		…
3195	}	3637	}
3196	}	3638	}
3197		3639
3198	/* simply recalculate all periodics */	3640	/* simply recalculate all periodics */
3199	/* TODO: maybe ensure that at least one event happens when jumping forward? */	3641	/* TODO: maybe ensure that at least one event happens when jumping forward? */
3200	static void noinline ecb_cold	3642	ecb_noinline ecb_cold
		3643	static void
3201	periodics_reschedule (EV_P)	3644	periodics_reschedule (EV_P)
3202	{	3645	{
3203	int i;	3646	int i;
3204		3647
3205	/* adjust periodics after time jump */	3648	/* adjust periodics after time jump */
…		…
3218	reheap (periodics, periodiccnt);	3661	reheap (periodics, periodiccnt);
3219	}	3662	}
3220	#endif	3663	#endif
3221		3664
3222	/* adjust all timers by a given offset */	3665	/* adjust all timers by a given offset */
3223	static void noinline ecb_cold	3666	ecb_noinline ecb_cold
		3667	static void
3224	timers_reschedule (EV_P_ ev_tstamp adjust)	3668	timers_reschedule (EV_P_ ev_tstamp adjust)
3225	{	3669	{
3226	int i;	3670	int i;
3227		3671
3228	for (i = 0; i < timercnt; ++i)	3672	for (i = 0; i < timercnt; ++i)
…		…
3237	/* also detect if there was a timejump, and act accordingly */	3681	/* also detect if there was a timejump, and act accordingly */
3238	inline_speed void	3682	inline_speed void
3239	time_update (EV_P_ ev_tstamp max_block)	3683	time_update (EV_P_ ev_tstamp max_block)
3240	{	3684	{
3241	#if EV_USE_MONOTONIC	3685	#if EV_USE_MONOTONIC
3242	if (expect_true (have_monotonic))	3686	if (ecb_expect_true (have_monotonic))
3243	{	3687	{
3244	int i;	3688	int i;
3245	ev_tstamp odiff = rtmn_diff;	3689	ev_tstamp odiff = rtmn_diff;
3246		3690
3247	mn_now = get_clock ();	3691	mn_now = get_clock ();
3248		3692
3249	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */	3693	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */
3250	/* interpolate in the meantime */	3694	/* interpolate in the meantime */
3251	if (expect_true (mn_now - now_floor < MIN_TIMEJUMP * .5))	3695	if (ecb_expect_true (mn_now - now_floor < EV_TS_CONST (MIN_TIMEJUMP * .5)))
3252	{	3696	{
3253	ev_rt_now = rtmn_diff + mn_now;	3697	ev_rt_now = rtmn_diff + mn_now;
3254	return;	3698	return;
3255	}	3699	}
3256		3700
…		…
3270	ev_tstamp diff;	3714	ev_tstamp diff;
3271	rtmn_diff = ev_rt_now - mn_now;	3715	rtmn_diff = ev_rt_now - mn_now;
3272		3716
3273	diff = odiff - rtmn_diff;	3717	diff = odiff - rtmn_diff;
3274		3718
3275	if (expect_true ((diff < 0. ? -diff : diff) < MIN_TIMEJUMP))	3719	if (ecb_expect_true ((diff < EV_TS_CONST (0.) ? -diff : diff) < EV_TS_CONST (MIN_TIMEJUMP)))
3276	return; /* all is well */	3720	return; /* all is well */
3277		3721
3278	ev_rt_now = ev_time ();	3722	ev_rt_now = ev_time ();
3279	mn_now = get_clock ();	3723	mn_now = get_clock ();
3280	now_floor = mn_now;	3724	now_floor = mn_now;
…		…
3289	else	3733	else
3290	#endif	3734	#endif
3291	{	3735	{
3292	ev_rt_now = ev_time ();	3736	ev_rt_now = ev_time ();
3293		3737
3294	if (expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + MIN_TIMEJUMP))	3738	if (ecb_expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + EV_TS_CONST (MIN_TIMEJUMP)))
3295	{	3739	{
3296	/* adjust timers. this is easy, as the offset is the same for all of them */	3740	/* adjust timers. this is easy, as the offset is the same for all of them */
3297	timers_reschedule (EV_A_ ev_rt_now - mn_now);	3741	timers_reschedule (EV_A_ ev_rt_now - mn_now);
3298	#if EV_PERIODIC_ENABLE	3742	#if EV_PERIODIC_ENABLE
3299	periodics_reschedule (EV_A);	3743	periodics_reschedule (EV_A);
…		…
3322	#if EV_VERIFY >= 2	3766	#if EV_VERIFY >= 2
3323	ev_verify (EV_A);	3767	ev_verify (EV_A);
3324	#endif	3768	#endif
3325		3769
3326	#ifndef _WIN32	3770	#ifndef _WIN32
3327	if (expect_false (curpid)) /* penalise the forking check even more */	3771	if (ecb_expect_false (curpid)) /* penalise the forking check even more */
3328	if (expect_false (getpid () != curpid))	3772	if (ecb_expect_false (getpid () != curpid))
3329	{	3773	{
3330	curpid = getpid ();	3774	curpid = getpid ();
3331	postfork = 1;	3775	postfork = 1;
3332	}	3776	}
3333	#endif	3777	#endif
3334		3778
3335	#if EV_FORK_ENABLE	3779	#if EV_FORK_ENABLE
3336	/* we might have forked, so queue fork handlers */	3780	/* we might have forked, so queue fork handlers */
3337	if (expect_false (postfork))	3781	if (ecb_expect_false (postfork))
3338	if (forkcnt)	3782	if (forkcnt)
3339	{	3783	{
3340	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);	3784	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);
3341	EV_INVOKE_PENDING;	3785	EV_INVOKE_PENDING;
3342	}	3786	}
3343	#endif	3787	#endif
3344		3788
3345	#if EV_PREPARE_ENABLE	3789	#if EV_PREPARE_ENABLE
3346	/* queue prepare watchers (and execute them) */	3790	/* queue prepare watchers (and execute them) */
3347	if (expect_false (preparecnt))	3791	if (ecb_expect_false (preparecnt))
3348	{	3792	{
3349	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);	3793	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);
3350	EV_INVOKE_PENDING;	3794	EV_INVOKE_PENDING;
3351	}	3795	}
3352	#endif	3796	#endif
3353		3797
3354	if (expect_false (loop_done))	3798	if (ecb_expect_false (loop_done))
3355	break;	3799	break;
3356		3800
3357	/* we might have forked, so reify kernel state if necessary */	3801	/* we might have forked, so reify kernel state if necessary */
3358	if (expect_false (postfork))	3802	if (ecb_expect_false (postfork))
3359	loop_fork (EV_A);	3803	loop_fork (EV_A);
3360		3804
3361	/* update fd-related kernel structures */	3805	/* update fd-related kernel structures */
3362	fd_reify (EV_A);	3806	fd_reify (EV_A);
3363		3807
…		…
3368		3812
3369	/* remember old timestamp for io_blocktime calculation */	3813	/* remember old timestamp for io_blocktime calculation */
3370	ev_tstamp prev_mn_now = mn_now;	3814	ev_tstamp prev_mn_now = mn_now;
3371		3815
3372	/* update time to cancel out callback processing overhead */	3816	/* update time to cancel out callback processing overhead */
3373	time_update (EV_A_ 1e100);	3817	time_update (EV_A_ EV_TS_CONST (EV_TSTAMP_HUGE));
3374		3818
3375	/* from now on, we want a pipe-wake-up */	3819	/* from now on, we want a pipe-wake-up */
3376	pipe_write_wanted = 1;	3820	pipe_write_wanted = 1;
3377		3821
3378	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */	3822	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */
3379		3823
3380	if (expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))	3824	if (ecb_expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))
3381	{	3825	{
3382	waittime = MAX_BLOCKTIME;	3826	waittime = EV_TS_CONST (MAX_BLOCKTIME);
3383		3827
3384	if (timercnt)	3828	if (timercnt)
3385	{	3829	{
3386	ev_tstamp to = ANHE_at (timers [HEAP0]) - mn_now;	3830	ev_tstamp to = ANHE_at (timers [HEAP0]) - mn_now;
3387	if (waittime > to) waittime = to;	3831	if (waittime > to) waittime = to;
…		…
3394	if (waittime > to) waittime = to;	3838	if (waittime > to) waittime = to;
3395	}	3839	}
3396	#endif	3840	#endif
3397		3841
3398	/* don't let timeouts decrease the waittime below timeout_blocktime */	3842	/* don't let timeouts decrease the waittime below timeout_blocktime */
3399	if (expect_false (waittime < timeout_blocktime))	3843	if (ecb_expect_false (waittime < timeout_blocktime))
3400	waittime = timeout_blocktime;	3844	waittime = timeout_blocktime;
3401		3845
3402	/* at this point, we NEED to wait, so we have to ensure */	3846	/* at this point, we NEED to wait, so we have to ensure */
3403	/* to pass a minimum nonzero value to the backend */	3847	/* to pass a minimum nonzero value to the backend */
3404	if (expect_false (waittime < backend_mintime))	3848	if (ecb_expect_false (waittime < backend_mintime))
3405	waittime = backend_mintime;	3849	waittime = backend_mintime;
3406		3850
3407	/* extra check because io_blocktime is commonly 0 */	3851	/* extra check because io_blocktime is commonly 0 */
3408	if (expect_false (io_blocktime))	3852	if (ecb_expect_false (io_blocktime))
3409	{	3853	{
3410	sleeptime = io_blocktime - (mn_now - prev_mn_now);	3854	sleeptime = io_blocktime - (mn_now - prev_mn_now);
3411		3855
3412	if (sleeptime > waittime - backend_mintime)	3856	if (sleeptime > waittime - backend_mintime)
3413	sleeptime = waittime - backend_mintime;	3857	sleeptime = waittime - backend_mintime;
3414		3858
3415	if (expect_true (sleeptime > 0.))	3859	if (ecb_expect_true (sleeptime > EV_TS_CONST (0.)))
3416	{	3860	{
3417	ev_sleep (sleeptime);	3861	ev_sleep (sleeptime);
3418	waittime -= sleeptime;	3862	waittime -= sleeptime;
3419	}	3863	}
3420	}	3864	}
…		…
3434	{	3878	{
3435	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));	3879	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));
3436	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);	3880	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);
3437	}	3881	}
3438		3882
3439
3440	/* update ev_rt_now, do magic */	3883	/* update ev_rt_now, do magic */
3441	time_update (EV_A_ waittime + sleeptime);	3884	time_update (EV_A_ waittime + sleeptime);
3442	}	3885	}
3443		3886
3444	/* queue pending timers and reschedule them */	3887	/* queue pending timers and reschedule them */
…		…
3452	idle_reify (EV_A);	3895	idle_reify (EV_A);
3453	#endif	3896	#endif
3454		3897
3455	#if EV_CHECK_ENABLE	3898	#if EV_CHECK_ENABLE
3456	/* queue check watchers, to be executed first */	3899	/* queue check watchers, to be executed first */
3457	if (expect_false (checkcnt))	3900	if (ecb_expect_false (checkcnt))
3458	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);	3901	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);
3459	#endif	3902	#endif
3460		3903
3461	EV_INVOKE_PENDING;	3904	EV_INVOKE_PENDING;
3462	}	3905	}
3463	while (expect_true (	3906	while (ecb_expect_true (
3464	activecnt	3907	activecnt
3465	&& !loop_done	3908	&& !loop_done
3466	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))	3909	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))
3467	));	3910	));
3468		3911
…		…
3475		3918
3476	return activecnt;	3919	return activecnt;
3477	}	3920	}
3478		3921
3479	void	3922	void
3480	ev_break (EV_P_ int how) EV_THROW	3923	ev_break (EV_P_ int how) EV_NOEXCEPT
3481	{	3924	{
3482	loop_done = how;	3925	loop_done = how;
3483	}	3926	}
3484		3927
3485	void	3928	void
3486	ev_ref (EV_P) EV_THROW	3929	ev_ref (EV_P) EV_NOEXCEPT
3487	{	3930	{
3488	++activecnt;	3931	++activecnt;
3489	}	3932	}
3490		3933
3491	void	3934	void
3492	ev_unref (EV_P) EV_THROW	3935	ev_unref (EV_P) EV_NOEXCEPT
3493	{	3936	{
3494	--activecnt;	3937	--activecnt;
3495	}	3938	}
3496		3939
3497	void	3940	void
3498	ev_now_update (EV_P) EV_THROW	3941	ev_now_update (EV_P) EV_NOEXCEPT
3499	{	3942	{
3500	time_update (EV_A_ 1e100);	3943	time_update (EV_A_ EV_TSTAMP_HUGE);
3501	}	3944	}
3502		3945
3503	void	3946	void
3504	ev_suspend (EV_P) EV_THROW	3947	ev_suspend (EV_P) EV_NOEXCEPT
3505	{	3948	{
3506	ev_now_update (EV_A);	3949	ev_now_update (EV_A);
3507	}	3950	}
3508		3951
3509	void	3952	void
3510	ev_resume (EV_P) EV_THROW	3953	ev_resume (EV_P) EV_NOEXCEPT
3511	{	3954	{
3512	ev_tstamp mn_prev = mn_now;	3955	ev_tstamp mn_prev = mn_now;
3513		3956
3514	ev_now_update (EV_A);	3957	ev_now_update (EV_A);
3515	timers_reschedule (EV_A_ mn_now - mn_prev);	3958	timers_reschedule (EV_A_ mn_now - mn_prev);
…		…
3532	inline_size void	3975	inline_size void
3533	wlist_del (WL *head, WL elem)	3976	wlist_del (WL *head, WL elem)
3534	{	3977	{
3535	while (*head)	3978	while (*head)
3536	{	3979	{
3537	if (expect_true (*head == elem))	3980	if (ecb_expect_true (*head == elem))
3538	{	3981	{
3539	*head = elem->next;	3982	*head = elem->next;
3540	break;	3983	break;
3541	}	3984	}
3542		3985
…		…
3554	w->pending = 0;	3997	w->pending = 0;
3555	}	3998	}
3556	}	3999	}
3557		4000
3558	int	4001	int
3559	ev_clear_pending (EV_P_ void *w) EV_THROW	4002	ev_clear_pending (EV_P_ void *w) EV_NOEXCEPT
3560	{	4003	{
3561	W w_ = (W)w;	4004	W w_ = (W)w;
3562	int pending = w_->pending;	4005	int pending = w_->pending;
3563		4006
3564	if (expect_true (pending))	4007	if (ecb_expect_true (pending))
3565	{	4008	{
3566	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;	4009	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;
3567	p->w = (W)&pending_w;	4010	p->w = (W)&pending_w;
3568	w_->pending = 0;	4011	w_->pending = 0;
3569	return p->events;	4012	return p->events;
…		…
3596	w->active = 0;	4039	w->active = 0;
3597	}	4040	}
3598		4041
3599	/*****************************************************************************/	4042	/*****************************************************************************/
3600		4043
3601	void noinline	4044	ecb_noinline
		4045	void
3602	ev_io_start (EV_P_ ev_io *w) EV_THROW	4046	ev_io_start (EV_P_ ev_io *w) EV_NOEXCEPT
3603	{	4047	{
3604	int fd = w->fd;	4048	int fd = w->fd;
3605		4049
3606	if (expect_false (ev_is_active (w)))	4050	if (ecb_expect_false (ev_is_active (w)))
3607	return;	4051	return;
3608		4052
3609	assert (("libev: ev_io_start called with negative fd", fd >= 0));	4053	assert (("libev: ev_io_start called with negative fd", fd >= 0));
3610	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));	4054	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));
3611		4055
		4056	#if EV_VERIFY >= 2
		4057	assert (("libev: ev_io_start called on watcher with invalid fd", fd_valid (fd)));
		4058	#endif
3612	EV_FREQUENT_CHECK;	4059	EV_FREQUENT_CHECK;
3613		4060
3614	ev_start (EV_A_ (W)w, 1);	4061	ev_start (EV_A_ (W)w, 1);
3615	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_init_zero);	4062	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_needsize_zerofill);
3616	wlist_add (&anfds[fd].head, (WL)w);	4063	wlist_add (&anfds[fd].head, (WL)w);
3617		4064
3618	/* common bug, apparently */	4065	/* common bug, apparently */
3619	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));	4066	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));
3620		4067
…		…
3622	w->events &= ~EV__IOFDSET;	4069	w->events &= ~EV__IOFDSET;
3623		4070
3624	EV_FREQUENT_CHECK;	4071	EV_FREQUENT_CHECK;
3625	}	4072	}
3626		4073
3627	void noinline	4074	ecb_noinline
		4075	void
3628	ev_io_stop (EV_P_ ev_io *w) EV_THROW	4076	ev_io_stop (EV_P_ ev_io *w) EV_NOEXCEPT
3629	{	4077	{
3630	clear_pending (EV_A_ (W)w);	4078	clear_pending (EV_A_ (W)w);
3631	if (expect_false (!ev_is_active (w)))	4079	if (ecb_expect_false (!ev_is_active (w)))
3632	return;	4080	return;
3633		4081
3634	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));	4082	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));
3635		4083
		4084	#if EV_VERIFY >= 2
		4085	assert (("libev: ev_io_stop called on watcher with invalid fd", fd_valid (w->fd)));
		4086	#endif
3636	EV_FREQUENT_CHECK;	4087	EV_FREQUENT_CHECK;
3637		4088
3638	wlist_del (&anfds[w->fd].head, (WL)w);	4089	wlist_del (&anfds[w->fd].head, (WL)w);
3639	ev_stop (EV_A_ (W)w);	4090	ev_stop (EV_A_ (W)w);
3640		4091
3641	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);	4092	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);
3642		4093
3643	EV_FREQUENT_CHECK;	4094	EV_FREQUENT_CHECK;
3644	}	4095	}
3645		4096
3646	void noinline	4097	ecb_noinline
		4098	void
3647	ev_timer_start (EV_P_ ev_timer *w) EV_THROW	4099	ev_timer_start (EV_P_ ev_timer *w) EV_NOEXCEPT
3648	{	4100	{
3649	if (expect_false (ev_is_active (w)))	4101	if (ecb_expect_false (ev_is_active (w)))
3650	return;	4102	return;
3651		4103
3652	ev_at (w) += mn_now;	4104	ev_at (w) += mn_now;
3653		4105
3654	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));	4106	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));
3655		4107
3656	EV_FREQUENT_CHECK;	4108	EV_FREQUENT_CHECK;
3657		4109
3658	++timercnt;	4110	++timercnt;
3659	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);	4111	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);
3660	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, EMPTY2);	4112	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, array_needsize_noinit);
3661	ANHE_w (timers [ev_active (w)]) = (WT)w;	4113	ANHE_w (timers [ev_active (w)]) = (WT)w;
3662	ANHE_at_cache (timers [ev_active (w)]);	4114	ANHE_at_cache (timers [ev_active (w)]);
3663	upheap (timers, ev_active (w));	4115	upheap (timers, ev_active (w));
3664		4116
3665	EV_FREQUENT_CHECK;	4117	EV_FREQUENT_CHECK;
3666		4118
3667	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/	4119	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/
3668	}	4120	}
3669		4121
3670	void noinline	4122	ecb_noinline
		4123	void
3671	ev_timer_stop (EV_P_ ev_timer *w) EV_THROW	4124	ev_timer_stop (EV_P_ ev_timer *w) EV_NOEXCEPT
3672	{	4125	{
3673	clear_pending (EV_A_ (W)w);	4126	clear_pending (EV_A_ (W)w);
3674	if (expect_false (!ev_is_active (w)))	4127	if (ecb_expect_false (!ev_is_active (w)))
3675	return;	4128	return;
3676		4129
3677	EV_FREQUENT_CHECK;	4130	EV_FREQUENT_CHECK;
3678		4131
3679	{	4132	{
…		…
3681		4134
3682	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));	4135	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));
3683		4136
3684	--timercnt;	4137	--timercnt;
3685		4138
3686	if (expect_true (active < timercnt + HEAP0))	4139	if (ecb_expect_true (active < timercnt + HEAP0))
3687	{	4140	{
3688	timers [active] = timers [timercnt + HEAP0];	4141	timers [active] = timers [timercnt + HEAP0];
3689	adjustheap (timers, timercnt, active);	4142	adjustheap (timers, timercnt, active);
3690	}	4143	}
3691	}	4144	}
…		…
3695	ev_stop (EV_A_ (W)w);	4148	ev_stop (EV_A_ (W)w);
3696		4149
3697	EV_FREQUENT_CHECK;	4150	EV_FREQUENT_CHECK;
3698	}	4151	}
3699		4152
3700	void noinline	4153	ecb_noinline
		4154	void
3701	ev_timer_again (EV_P_ ev_timer *w) EV_THROW	4155	ev_timer_again (EV_P_ ev_timer *w) EV_NOEXCEPT
3702	{	4156	{
3703	EV_FREQUENT_CHECK;	4157	EV_FREQUENT_CHECK;
3704		4158
3705	clear_pending (EV_A_ (W)w);	4159	clear_pending (EV_A_ (W)w);
3706		4160
…		…
3723		4177
3724	EV_FREQUENT_CHECK;	4178	EV_FREQUENT_CHECK;
3725	}	4179	}
3726		4180
3727	ev_tstamp	4181	ev_tstamp
3728	ev_timer_remaining (EV_P_ ev_timer *w) EV_THROW	4182	ev_timer_remaining (EV_P_ ev_timer *w) EV_NOEXCEPT
3729	{	4183	{
3730	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);	4184	return ev_at (w) - (ev_is_active (w) ? mn_now : EV_TS_CONST (0.));
3731	}	4185	}
3732		4186
3733	#if EV_PERIODIC_ENABLE	4187	#if EV_PERIODIC_ENABLE
3734	void noinline	4188	ecb_noinline
		4189	void
3735	ev_periodic_start (EV_P_ ev_periodic *w) EV_THROW	4190	ev_periodic_start (EV_P_ ev_periodic *w) EV_NOEXCEPT
3736	{	4191	{
3737	if (expect_false (ev_is_active (w)))	4192	if (ecb_expect_false (ev_is_active (w)))
3738	return;	4193	return;
3739		4194
3740	if (w->reschedule_cb)	4195	if (w->reschedule_cb)
3741	ev_at (w) = w->reschedule_cb (w, ev_rt_now);	4196	ev_at (w) = w->reschedule_cb (w, ev_rt_now);
3742	else if (w->interval)	4197	else if (w->interval)
…		…
3749		4204
3750	EV_FREQUENT_CHECK;	4205	EV_FREQUENT_CHECK;
3751		4206
3752	++periodiccnt;	4207	++periodiccnt;
3753	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);	4208	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);
3754	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, EMPTY2);	4209	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, array_needsize_noinit);
3755	ANHE_w (periodics [ev_active (w)]) = (WT)w;	4210	ANHE_w (periodics [ev_active (w)]) = (WT)w;
3756	ANHE_at_cache (periodics [ev_active (w)]);	4211	ANHE_at_cache (periodics [ev_active (w)]);
3757	upheap (periodics, ev_active (w));	4212	upheap (periodics, ev_active (w));
3758		4213
3759	EV_FREQUENT_CHECK;	4214	EV_FREQUENT_CHECK;
3760		4215
3761	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/	4216	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/
3762	}	4217	}
3763		4218
3764	void noinline	4219	ecb_noinline
		4220	void
3765	ev_periodic_stop (EV_P_ ev_periodic *w) EV_THROW	4221	ev_periodic_stop (EV_P_ ev_periodic *w) EV_NOEXCEPT
3766	{	4222	{
3767	clear_pending (EV_A_ (W)w);	4223	clear_pending (EV_A_ (W)w);
3768	if (expect_false (!ev_is_active (w)))	4224	if (ecb_expect_false (!ev_is_active (w)))
3769	return;	4225	return;
3770		4226
3771	EV_FREQUENT_CHECK;	4227	EV_FREQUENT_CHECK;
3772		4228
3773	{	4229	{
…		…
3775		4231
3776	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));	4232	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));
3777		4233
3778	--periodiccnt;	4234	--periodiccnt;
3779		4235
3780	if (expect_true (active < periodiccnt + HEAP0))	4236	if (ecb_expect_true (active < periodiccnt + HEAP0))
3781	{	4237	{
3782	periodics [active] = periodics [periodiccnt + HEAP0];	4238	periodics [active] = periodics [periodiccnt + HEAP0];
3783	adjustheap (periodics, periodiccnt, active);	4239	adjustheap (periodics, periodiccnt, active);
3784	}	4240	}
3785	}	4241	}
…		…
3787	ev_stop (EV_A_ (W)w);	4243	ev_stop (EV_A_ (W)w);
3788		4244
3789	EV_FREQUENT_CHECK;	4245	EV_FREQUENT_CHECK;
3790	}	4246	}
3791		4247
3792	void noinline	4248	ecb_noinline
		4249	void
3793	ev_periodic_again (EV_P_ ev_periodic *w) EV_THROW	4250	ev_periodic_again (EV_P_ ev_periodic *w) EV_NOEXCEPT
3794	{	4251	{
3795	/* TODO: use adjustheap and recalculation */	4252	/* TODO: use adjustheap and recalculation */
3796	ev_periodic_stop (EV_A_ w);	4253	ev_periodic_stop (EV_A_ w);
3797	ev_periodic_start (EV_A_ w);	4254	ev_periodic_start (EV_A_ w);
3798	}	4255	}
…		…
3802	# define SA_RESTART 0	4259	# define SA_RESTART 0
3803	#endif	4260	#endif
3804		4261
3805	#if EV_SIGNAL_ENABLE	4262	#if EV_SIGNAL_ENABLE
3806		4263
3807	void noinline	4264	ecb_noinline
		4265	void
3808	ev_signal_start (EV_P_ ev_signal *w) EV_THROW	4266	ev_signal_start (EV_P_ ev_signal *w) EV_NOEXCEPT
3809	{	4267	{
3810	if (expect_false (ev_is_active (w)))	4268	if (ecb_expect_false (ev_is_active (w)))
3811	return;	4269	return;
3812		4270
3813	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));	4271	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));
3814		4272
3815	#if EV_MULTIPLICITY	4273	#if EV_MULTIPLICITY
…		…
3884	}	4342	}
3885		4343
3886	EV_FREQUENT_CHECK;	4344	EV_FREQUENT_CHECK;
3887	}	4345	}
3888		4346
3889	void noinline	4347	ecb_noinline
		4348	void
3890	ev_signal_stop (EV_P_ ev_signal *w) EV_THROW	4349	ev_signal_stop (EV_P_ ev_signal *w) EV_NOEXCEPT
3891	{	4350	{
3892	clear_pending (EV_A_ (W)w);	4351	clear_pending (EV_A_ (W)w);
3893	if (expect_false (!ev_is_active (w)))	4352	if (ecb_expect_false (!ev_is_active (w)))
3894	return;	4353	return;
3895		4354
3896	EV_FREQUENT_CHECK;	4355	EV_FREQUENT_CHECK;
3897		4356
3898	wlist_del (&signals [w->signum - 1].head, (WL)w);	4357	wlist_del (&signals [w->signum - 1].head, (WL)w);
…		…
3926	#endif	4385	#endif
3927		4386
3928	#if EV_CHILD_ENABLE	4387	#if EV_CHILD_ENABLE
3929		4388
3930	void	4389	void
3931	ev_child_start (EV_P_ ev_child *w) EV_THROW	4390	ev_child_start (EV_P_ ev_child *w) EV_NOEXCEPT
3932	{	4391	{
3933	#if EV_MULTIPLICITY	4392	#if EV_MULTIPLICITY
3934	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));	4393	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));
3935	#endif	4394	#endif
3936	if (expect_false (ev_is_active (w)))	4395	if (ecb_expect_false (ev_is_active (w)))
3937	return;	4396	return;
3938		4397
3939	EV_FREQUENT_CHECK;	4398	EV_FREQUENT_CHECK;
3940		4399
3941	ev_start (EV_A_ (W)w, 1);	4400	ev_start (EV_A_ (W)w, 1);
…		…
3943		4402
3944	EV_FREQUENT_CHECK;	4403	EV_FREQUENT_CHECK;
3945	}	4404	}
3946		4405
3947	void	4406	void
3948	ev_child_stop (EV_P_ ev_child *w) EV_THROW	4407	ev_child_stop (EV_P_ ev_child *w) EV_NOEXCEPT
3949	{	4408	{
3950	clear_pending (EV_A_ (W)w);	4409	clear_pending (EV_A_ (W)w);
3951	if (expect_false (!ev_is_active (w)))	4410	if (ecb_expect_false (!ev_is_active (w)))
3952	return;	4411	return;
3953		4412
3954	EV_FREQUENT_CHECK;	4413	EV_FREQUENT_CHECK;
3955		4414
3956	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);	4415	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);
…		…
3970		4429
3971	#define DEF_STAT_INTERVAL 5.0074891	4430	#define DEF_STAT_INTERVAL 5.0074891
3972	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */	4431	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */
3973	#define MIN_STAT_INTERVAL 0.1074891	4432	#define MIN_STAT_INTERVAL 0.1074891
3974		4433
3975	static void noinline stat_timer_cb (EV_P_ ev_timer *w_, int revents);	4434	ecb_noinline static void stat_timer_cb (EV_P_ ev_timer *w_, int revents);
3976		4435
3977	#if EV_USE_INOTIFY	4436	#if EV_USE_INOTIFY
3978		4437
3979	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */	4438	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */
3980	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)	4439	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)
3981		4440
3982	static void noinline	4441	ecb_noinline
		4442	static void
3983	infy_add (EV_P_ ev_stat *w)	4443	infy_add (EV_P_ ev_stat *w)
3984	{	4444	{
3985	w->wd = inotify_add_watch (fs_fd, w->path,	4445	w->wd = inotify_add_watch (fs_fd, w->path,
3986	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY	4446	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY
3987	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO	4447	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO
…		…
4051	if (ev_is_active (&w->timer)) ev_ref (EV_A);	4511	if (ev_is_active (&w->timer)) ev_ref (EV_A);
4052	ev_timer_again (EV_A_ &w->timer);	4512	ev_timer_again (EV_A_ &w->timer);
4053	if (ev_is_active (&w->timer)) ev_unref (EV_A);	4513	if (ev_is_active (&w->timer)) ev_unref (EV_A);
4054	}	4514	}
4055		4515
4056	static void noinline	4516	ecb_noinline
		4517	static void
4057	infy_del (EV_P_ ev_stat *w)	4518	infy_del (EV_P_ ev_stat *w)
4058	{	4519	{
4059	int slot;	4520	int slot;
4060	int wd = w->wd;	4521	int wd = w->wd;
4061		4522
…		…
4068		4529
4069	/* remove this watcher, if others are watching it, they will rearm */	4530	/* remove this watcher, if others are watching it, they will rearm */
4070	inotify_rm_watch (fs_fd, wd);	4531	inotify_rm_watch (fs_fd, wd);
4071	}	4532	}
4072		4533
4073	static void noinline	4534	ecb_noinline
		4535	static void
4074	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)	4536	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)
4075	{	4537	{
4076	if (slot < 0)	4538	if (slot < 0)
4077	/* overflow, need to check for all hash slots */	4539	/* overflow, need to check for all hash slots */
4078	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)	4540	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)
…		…
4114	infy_wd (EV_A_ ev->wd, ev->wd, ev);	4576	infy_wd (EV_A_ ev->wd, ev->wd, ev);
4115	ofs += sizeof (struct inotify_event) + ev->len;	4577	ofs += sizeof (struct inotify_event) + ev->len;
4116	}	4578	}
4117	}	4579	}
4118		4580
4119	inline_size void ecb_cold	4581	inline_size ecb_cold
		4582	void
4120	ev_check_2625 (EV_P)	4583	ev_check_2625 (EV_P)
4121	{	4584	{
4122	/* kernels < 2.6.25 are borked	4585	/* kernels < 2.6.25 are borked
4123	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html	4586	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html
4124	*/	4587	*/
…		…
4214	#else	4677	#else
4215	# define EV_LSTAT(p,b) lstat (p, b)	4678	# define EV_LSTAT(p,b) lstat (p, b)
4216	#endif	4679	#endif
4217		4680
4218	void	4681	void
4219	ev_stat_stat (EV_P_ ev_stat *w) EV_THROW	4682	ev_stat_stat (EV_P_ ev_stat *w) EV_NOEXCEPT
4220	{	4683	{
4221	if (lstat (w->path, &w->attr) < 0)	4684	if (lstat (w->path, &w->attr) < 0)
4222	w->attr.st_nlink = 0;	4685	w->attr.st_nlink = 0;
4223	else if (!w->attr.st_nlink)	4686	else if (!w->attr.st_nlink)
4224	w->attr.st_nlink = 1;	4687	w->attr.st_nlink = 1;
4225	}	4688	}
4226		4689
4227	static void noinline	4690	ecb_noinline
		4691	static void
4228	stat_timer_cb (EV_P_ ev_timer *w_, int revents)	4692	stat_timer_cb (EV_P_ ev_timer *w_, int revents)
4229	{	4693	{
4230	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));	4694	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));
4231		4695
4232	ev_statdata prev = w->attr;	4696	ev_statdata prev = w->attr;
…		…
4263	ev_feed_event (EV_A_ w, EV_STAT);	4727	ev_feed_event (EV_A_ w, EV_STAT);
4264	}	4728	}
4265	}	4729	}
4266		4730
4267	void	4731	void
4268	ev_stat_start (EV_P_ ev_stat *w) EV_THROW	4732	ev_stat_start (EV_P_ ev_stat *w) EV_NOEXCEPT
4269	{	4733	{
4270	if (expect_false (ev_is_active (w)))	4734	if (ecb_expect_false (ev_is_active (w)))
4271	return;	4735	return;
4272		4736
4273	ev_stat_stat (EV_A_ w);	4737	ev_stat_stat (EV_A_ w);
4274		4738
4275	if (w->interval < MIN_STAT_INTERVAL && w->interval)	4739	if (w->interval < MIN_STAT_INTERVAL && w->interval)
…		…
4294		4758
4295	EV_FREQUENT_CHECK;	4759	EV_FREQUENT_CHECK;
4296	}	4760	}
4297		4761
4298	void	4762	void
4299	ev_stat_stop (EV_P_ ev_stat *w) EV_THROW	4763	ev_stat_stop (EV_P_ ev_stat *w) EV_NOEXCEPT
4300	{	4764	{
4301	clear_pending (EV_A_ (W)w);	4765	clear_pending (EV_A_ (W)w);
4302	if (expect_false (!ev_is_active (w)))	4766	if (ecb_expect_false (!ev_is_active (w)))
4303	return;	4767	return;
4304		4768
4305	EV_FREQUENT_CHECK;	4769	EV_FREQUENT_CHECK;
4306		4770
4307	#if EV_USE_INOTIFY	4771	#if EV_USE_INOTIFY
…		…
4320	}	4784	}
4321	#endif	4785	#endif
4322		4786
4323	#if EV_IDLE_ENABLE	4787	#if EV_IDLE_ENABLE
4324	void	4788	void
4325	ev_idle_start (EV_P_ ev_idle *w) EV_THROW	4789	ev_idle_start (EV_P_ ev_idle *w) EV_NOEXCEPT
4326	{	4790	{
4327	if (expect_false (ev_is_active (w)))	4791	if (ecb_expect_false (ev_is_active (w)))
4328	return;	4792	return;
4329		4793
4330	pri_adjust (EV_A_ (W)w);	4794	pri_adjust (EV_A_ (W)w);
4331		4795
4332	EV_FREQUENT_CHECK;	4796	EV_FREQUENT_CHECK;
…		…
4335	int active = ++idlecnt [ABSPRI (w)];	4799	int active = ++idlecnt [ABSPRI (w)];
4336		4800
4337	++idleall;	4801	++idleall;
4338	ev_start (EV_A_ (W)w, active);	4802	ev_start (EV_A_ (W)w, active);
4339		4803
4340	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, EMPTY2);	4804	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, array_needsize_noinit);
4341	idles [ABSPRI (w)][active - 1] = w;	4805	idles [ABSPRI (w)][active - 1] = w;
4342	}	4806	}
4343		4807
4344	EV_FREQUENT_CHECK;	4808	EV_FREQUENT_CHECK;
4345	}	4809	}
4346		4810
4347	void	4811	void
4348	ev_idle_stop (EV_P_ ev_idle *w) EV_THROW	4812	ev_idle_stop (EV_P_ ev_idle *w) EV_NOEXCEPT
4349	{	4813	{
4350	clear_pending (EV_A_ (W)w);	4814	clear_pending (EV_A_ (W)w);
4351	if (expect_false (!ev_is_active (w)))	4815	if (ecb_expect_false (!ev_is_active (w)))
4352	return;	4816	return;
4353		4817
4354	EV_FREQUENT_CHECK;	4818	EV_FREQUENT_CHECK;
4355		4819
4356	{	4820	{
…		…
4367	}	4831	}
4368	#endif	4832	#endif
4369		4833
4370	#if EV_PREPARE_ENABLE	4834	#if EV_PREPARE_ENABLE
4371	void	4835	void
4372	ev_prepare_start (EV_P_ ev_prepare *w) EV_THROW	4836	ev_prepare_start (EV_P_ ev_prepare *w) EV_NOEXCEPT
4373	{	4837	{
4374	if (expect_false (ev_is_active (w)))	4838	if (ecb_expect_false (ev_is_active (w)))
4375	return;	4839	return;
4376		4840
4377	EV_FREQUENT_CHECK;	4841	EV_FREQUENT_CHECK;
4378		4842
4379	ev_start (EV_A_ (W)w, ++preparecnt);	4843	ev_start (EV_A_ (W)w, ++preparecnt);
4380	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, EMPTY2);	4844	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, array_needsize_noinit);
4381	prepares [preparecnt - 1] = w;	4845	prepares [preparecnt - 1] = w;
4382		4846
4383	EV_FREQUENT_CHECK;	4847	EV_FREQUENT_CHECK;
4384	}	4848	}
4385		4849
4386	void	4850	void
4387	ev_prepare_stop (EV_P_ ev_prepare *w) EV_THROW	4851	ev_prepare_stop (EV_P_ ev_prepare *w) EV_NOEXCEPT
4388	{	4852	{
4389	clear_pending (EV_A_ (W)w);	4853	clear_pending (EV_A_ (W)w);
4390	if (expect_false (!ev_is_active (w)))	4854	if (ecb_expect_false (!ev_is_active (w)))
4391	return;	4855	return;
4392		4856
4393	EV_FREQUENT_CHECK;	4857	EV_FREQUENT_CHECK;
4394		4858
4395	{	4859	{
…		…
4405	}	4869	}
4406	#endif	4870	#endif
4407		4871
4408	#if EV_CHECK_ENABLE	4872	#if EV_CHECK_ENABLE
4409	void	4873	void
4410	ev_check_start (EV_P_ ev_check *w) EV_THROW	4874	ev_check_start (EV_P_ ev_check *w) EV_NOEXCEPT
4411	{	4875	{
4412	if (expect_false (ev_is_active (w)))	4876	if (ecb_expect_false (ev_is_active (w)))
4413	return;	4877	return;
4414		4878
4415	EV_FREQUENT_CHECK;	4879	EV_FREQUENT_CHECK;
4416		4880
4417	ev_start (EV_A_ (W)w, ++checkcnt);	4881	ev_start (EV_A_ (W)w, ++checkcnt);
4418	array_needsize (ev_check *, checks, checkmax, checkcnt, EMPTY2);	4882	array_needsize (ev_check *, checks, checkmax, checkcnt, array_needsize_noinit);
4419	checks [checkcnt - 1] = w;	4883	checks [checkcnt - 1] = w;
4420		4884
4421	EV_FREQUENT_CHECK;	4885	EV_FREQUENT_CHECK;
4422	}	4886	}
4423		4887
4424	void	4888	void
4425	ev_check_stop (EV_P_ ev_check *w) EV_THROW	4889	ev_check_stop (EV_P_ ev_check *w) EV_NOEXCEPT
4426	{	4890	{
4427	clear_pending (EV_A_ (W)w);	4891	clear_pending (EV_A_ (W)w);
4428	if (expect_false (!ev_is_active (w)))	4892	if (ecb_expect_false (!ev_is_active (w)))
4429	return;	4893	return;
4430		4894
4431	EV_FREQUENT_CHECK;	4895	EV_FREQUENT_CHECK;
4432		4896
4433	{	4897	{
…		…
4442	EV_FREQUENT_CHECK;	4906	EV_FREQUENT_CHECK;
4443	}	4907	}
4444	#endif	4908	#endif
4445		4909
4446	#if EV_EMBED_ENABLE	4910	#if EV_EMBED_ENABLE
4447	void noinline	4911	ecb_noinline
		4912	void
4448	ev_embed_sweep (EV_P_ ev_embed *w) EV_THROW	4913	ev_embed_sweep (EV_P_ ev_embed *w) EV_NOEXCEPT
4449	{	4914	{
4450	ev_run (w->other, EVRUN_NOWAIT);	4915	ev_run (w->other, EVRUN_NOWAIT);
4451	}	4916	}
4452		4917
4453	static void	4918	static void
…		…
4501	ev_idle_stop (EV_A_ idle);	4966	ev_idle_stop (EV_A_ idle);
4502	}	4967	}
4503	#endif	4968	#endif
4504		4969
4505	void	4970	void
4506	ev_embed_start (EV_P_ ev_embed *w) EV_THROW	4971	ev_embed_start (EV_P_ ev_embed *w) EV_NOEXCEPT
4507	{	4972	{
4508	if (expect_false (ev_is_active (w)))	4973	if (ecb_expect_false (ev_is_active (w)))
4509	return;	4974	return;
4510		4975
4511	{	4976	{
4512	EV_P = w->other;	4977	EV_P = w->other;
4513	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));	4978	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));
…		…
4532		4997
4533	EV_FREQUENT_CHECK;	4998	EV_FREQUENT_CHECK;
4534	}	4999	}
4535		5000
4536	void	5001	void
4537	ev_embed_stop (EV_P_ ev_embed *w) EV_THROW	5002	ev_embed_stop (EV_P_ ev_embed *w) EV_NOEXCEPT
4538	{	5003	{
4539	clear_pending (EV_A_ (W)w);	5004	clear_pending (EV_A_ (W)w);
4540	if (expect_false (!ev_is_active (w)))	5005	if (ecb_expect_false (!ev_is_active (w)))
4541	return;	5006	return;
4542		5007
4543	EV_FREQUENT_CHECK;	5008	EV_FREQUENT_CHECK;
4544		5009
4545	ev_io_stop (EV_A_ &w->io);	5010	ev_io_stop (EV_A_ &w->io);
…		…
4552	}	5017	}
4553	#endif	5018	#endif
4554		5019
4555	#if EV_FORK_ENABLE	5020	#if EV_FORK_ENABLE
4556	void	5021	void
4557	ev_fork_start (EV_P_ ev_fork *w) EV_THROW	5022	ev_fork_start (EV_P_ ev_fork *w) EV_NOEXCEPT
4558	{	5023	{
4559	if (expect_false (ev_is_active (w)))	5024	if (ecb_expect_false (ev_is_active (w)))
4560	return;	5025	return;
4561		5026
4562	EV_FREQUENT_CHECK;	5027	EV_FREQUENT_CHECK;
4563		5028
4564	ev_start (EV_A_ (W)w, ++forkcnt);	5029	ev_start (EV_A_ (W)w, ++forkcnt);
4565	array_needsize (ev_fork *, forks, forkmax, forkcnt, EMPTY2);	5030	array_needsize (ev_fork *, forks, forkmax, forkcnt, array_needsize_noinit);
4566	forks [forkcnt - 1] = w;	5031	forks [forkcnt - 1] = w;
4567		5032
4568	EV_FREQUENT_CHECK;	5033	EV_FREQUENT_CHECK;
4569	}	5034	}
4570		5035
4571	void	5036	void
4572	ev_fork_stop (EV_P_ ev_fork *w) EV_THROW	5037	ev_fork_stop (EV_P_ ev_fork *w) EV_NOEXCEPT
4573	{	5038	{
4574	clear_pending (EV_A_ (W)w);	5039	clear_pending (EV_A_ (W)w);
4575	if (expect_false (!ev_is_active (w)))	5040	if (ecb_expect_false (!ev_is_active (w)))
4576	return;	5041	return;
4577		5042
4578	EV_FREQUENT_CHECK;	5043	EV_FREQUENT_CHECK;
4579		5044
4580	{	5045	{
…		…
4590	}	5055	}
4591	#endif	5056	#endif
4592		5057
4593	#if EV_CLEANUP_ENABLE	5058	#if EV_CLEANUP_ENABLE
4594	void	5059	void
4595	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_THROW	5060	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4596	{	5061	{
4597	if (expect_false (ev_is_active (w)))	5062	if (ecb_expect_false (ev_is_active (w)))
4598	return;	5063	return;
4599		5064
4600	EV_FREQUENT_CHECK;	5065	EV_FREQUENT_CHECK;
4601		5066
4602	ev_start (EV_A_ (W)w, ++cleanupcnt);	5067	ev_start (EV_A_ (W)w, ++cleanupcnt);
4603	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, EMPTY2);	5068	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, array_needsize_noinit);
4604	cleanups [cleanupcnt - 1] = w;	5069	cleanups [cleanupcnt - 1] = w;
4605		5070
4606	/* cleanup watchers should never keep a refcount on the loop */	5071	/* cleanup watchers should never keep a refcount on the loop */
4607	ev_unref (EV_A);	5072	ev_unref (EV_A);
4608	EV_FREQUENT_CHECK;	5073	EV_FREQUENT_CHECK;
4609	}	5074	}
4610		5075
4611	void	5076	void
4612	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_THROW	5077	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4613	{	5078	{
4614	clear_pending (EV_A_ (W)w);	5079	clear_pending (EV_A_ (W)w);
4615	if (expect_false (!ev_is_active (w)))	5080	if (ecb_expect_false (!ev_is_active (w)))
4616	return;	5081	return;
4617		5082
4618	EV_FREQUENT_CHECK;	5083	EV_FREQUENT_CHECK;
4619	ev_ref (EV_A);	5084	ev_ref (EV_A);
4620		5085
…		…
4631	}	5096	}
4632	#endif	5097	#endif
4633		5098
4634	#if EV_ASYNC_ENABLE	5099	#if EV_ASYNC_ENABLE
4635	void	5100	void
4636	ev_async_start (EV_P_ ev_async *w) EV_THROW	5101	ev_async_start (EV_P_ ev_async *w) EV_NOEXCEPT
4637	{	5102	{
4638	if (expect_false (ev_is_active (w)))	5103	if (ecb_expect_false (ev_is_active (w)))
4639	return;	5104	return;
4640		5105
4641	w->sent = 0;	5106	w->sent = 0;
4642		5107
4643	evpipe_init (EV_A);	5108	evpipe_init (EV_A);
4644		5109
4645	EV_FREQUENT_CHECK;	5110	EV_FREQUENT_CHECK;
4646		5111
4647	ev_start (EV_A_ (W)w, ++asynccnt);	5112	ev_start (EV_A_ (W)w, ++asynccnt);
4648	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, EMPTY2);	5113	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, array_needsize_noinit);
4649	asyncs [asynccnt - 1] = w;	5114	asyncs [asynccnt - 1] = w;
4650		5115
4651	EV_FREQUENT_CHECK;	5116	EV_FREQUENT_CHECK;
4652	}	5117	}
4653		5118
4654	void	5119	void
4655	ev_async_stop (EV_P_ ev_async *w) EV_THROW	5120	ev_async_stop (EV_P_ ev_async *w) EV_NOEXCEPT
4656	{	5121	{
4657	clear_pending (EV_A_ (W)w);	5122	clear_pending (EV_A_ (W)w);
4658	if (expect_false (!ev_is_active (w)))	5123	if (ecb_expect_false (!ev_is_active (w)))
4659	return;	5124	return;
4660		5125
4661	EV_FREQUENT_CHECK;	5126	EV_FREQUENT_CHECK;
4662		5127
4663	{	5128	{
…		…
4671		5136
4672	EV_FREQUENT_CHECK;	5137	EV_FREQUENT_CHECK;
4673	}	5138	}
4674		5139
4675	void	5140	void
4676	ev_async_send (EV_P_ ev_async *w) EV_THROW	5141	ev_async_send (EV_P_ ev_async *w) EV_NOEXCEPT
4677	{	5142	{
4678	w->sent = 1;	5143	w->sent = 1;
4679	evpipe_write (EV_A_ &async_pending);	5144	evpipe_write (EV_A_ &async_pending);
4680	}	5145	}
4681	#endif	5146	#endif
…		…
4718		5183
4719	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));	5184	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));
4720	}	5185	}
4721		5186
4722	void	5187	void
4723	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_THROW	5188	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_NOEXCEPT
4724	{	5189	{
4725	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));	5190	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));
4726
4727	if (expect_false (!once))
4728	{
4729	cb (EV_ERROR | EV_READ | EV_WRITE | EV_TIMER, arg);
4730	return;
4731	}
4732		5191
4733	once->cb = cb;	5192	once->cb = cb;
4734	once->arg = arg;	5193	once->arg = arg;
4735		5194
4736	ev_init (&once->io, once_cb_io);	5195	ev_init (&once->io, once_cb_io);
…		…
4749	}	5208	}
4750		5209
4751	/*****************************************************************************/	5210	/*****************************************************************************/
4752		5211
4753	#if EV_WALK_ENABLE	5212	#if EV_WALK_ENABLE
4754	void ecb_cold	5213	ecb_cold
		5214	void
4755	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_THROW	5215	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_NOEXCEPT
4756	{	5216	{
4757	int i, j;	5217	int i, j;
4758	ev_watcher_list *wl, *wn;	5218	ev_watcher_list *wl, *wn;
4759		5219
4760	if (types & (EV_IO | EV_EMBED))	5220	if (types & (EV_IO | EV_EMBED))

Diff Legend

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