ViewVC Help

View File | Revision Log | Show Annotations | Download File

/cvs/libev/ev.c

Comparing libev/ev.c (file contents):
Revision 1.466 by root, Tue Mar 25 19:26:42 2014 UTC vs.
Revision 1.496 by root, Mon Jun 24 22:27:29 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
309	#ifndef EV_USE_INOTIFY	337	#ifndef EV_USE_INOTIFY
310	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))	338	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))
311	# define EV_USE_INOTIFY EV_FEATURE_OS	339	# define EV_USE_INOTIFY EV_FEATURE_OS
312	# else	340	# else
313	# define EV_USE_INOTIFY 0	341	# define EV_USE_INOTIFY 0
…		…
354		382
355	#ifndef EV_HEAP_CACHE_AT	383	#ifndef EV_HEAP_CACHE_AT
356	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA	384	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA
357	#endif	385	#endif
358		386
359	#ifdef ANDROID	387	#ifdef __ANDROID__
360	/* supposedly, android doesn't typedef fd_mask */	388	/* supposedly, android doesn't typedef fd_mask */
361	# undef EV_USE_SELECT	389	# undef EV_USE_SELECT
362	# define EV_USE_SELECT 0	390	# define EV_USE_SELECT 0
363	/* supposedly, we need to include syscall.h, not sys/syscall.h, so just disable */	391	/* supposedly, we need to include syscall.h, not sys/syscall.h, so just disable */
364	# undef EV_USE_CLOCK_SYSCALL	392	# undef EV_USE_CLOCK_SYSCALL
…		…
405		433
406	#if !EV_USE_NANOSLEEP	434	#if !EV_USE_NANOSLEEP
407	/* hp-ux has it in sys/time.h, which we unconditionally include above */	435	/* hp-ux has it in sys/time.h, which we unconditionally include above */
408	# if !defined _WIN32 && !defined __hpux	436	# if !defined _WIN32 && !defined __hpux
409	# include <sys/select.h>	437	# include <sys/select.h>
		438	# endif
		439	#endif
		440
		441	#if EV_USE_LINUXAIO
		442	# include <sys/syscall.h>
		443	# if !SYS_io_getevents || !EV_USE_EPOLL /* ev_linxaio uses ev_poll.c:ev_epoll_create */
		444	# undef EV_USE_LINUXAIO
		445	# define EV_USE_LINUXAIO 0
410	# endif	446	# endif
411	#endif	447	#endif
412		448
413	#if EV_USE_INOTIFY	449	#if EV_USE_INOTIFY
414	# include <sys/statfs.h>	450	# include <sys/statfs.h>
…		…
482	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */	518	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */
483	/* ECB.H BEGIN */	519	/* ECB.H BEGIN */
484	/*	520	/*
485	* libecb - http://software.schmorp.de/pkg/libecb	521	* libecb - http://software.schmorp.de/pkg/libecb
486	*	522	*
487	* Copyright (©) 2009-2014 Marc Alexander Lehmann <libecb@schmorp.de>	523	* Copyright (©) 2009-2015 Marc Alexander Lehmann <libecb@schmorp.de>
488	* Copyright (©) 2011 Emanuele Giaquinta	524	* Copyright (©) 2011 Emanuele Giaquinta
489	* All rights reserved.	525	* All rights reserved.
490	*	526	*
491	* Redistribution and use in source and binary forms, with or without modifica-	527	* Redistribution and use in source and binary forms, with or without modifica-
492	* tion, are permitted provided that the following conditions are met:	528	* tion, are permitted provided that the following conditions are met:
…		…
506	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;	542	* PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR PROFITS;
507	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,	543	* OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY,
508	* WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING NEGLIGENCE OR OTH-	544	* 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	545	* ERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED
510	* OF THE POSSIBILITY OF SUCH DAMAGE.	546	* OF THE POSSIBILITY OF SUCH DAMAGE.
		547	*
		548	* Alternatively, the contents of this file may be used under the terms of
		549	* the GNU General Public License ("GPL") version 2 or any later version,
		550	* in which case the provisions of the GPL are applicable instead of
		551	* the above. If you wish to allow the use of your version of this file
		552	* only under the terms of the GPL and not to allow others to use your
		553	* version of this file under the BSD license, indicate your decision
		554	* by deleting the provisions above and replace them with the notice
		555	* and other provisions required by the GPL. If you do not delete the
		556	* provisions above, a recipient may use your version of this file under
		557	* either the BSD or the GPL.
511	*/	558	*/
512		559
513	#ifndef ECB_H	560	#ifndef ECB_H
514	#define ECB_H	561	#define ECB_H
515		562
516	/* 16 bits major, 16 bits minor */	563	/* 16 bits major, 16 bits minor */
517	#define ECB_VERSION 0x00010003	564	#define ECB_VERSION 0x00010006
518		565
519	#ifdef _WIN32	566	#ifdef _WIN32
520	typedef signed char int8_t;	567	typedef signed char int8_t;
521	typedef unsigned char uint8_t;	568	typedef unsigned char uint8_t;
522	typedef signed short int16_t;	569	typedef signed short int16_t;
…		…
539	typedef uint32_t uintptr_t;	586	typedef uint32_t uintptr_t;
540	typedef int32_t intptr_t;	587	typedef int32_t intptr_t;
541	#endif	588	#endif
542	#else	589	#else
543	#include <inttypes.h>	590	#include <inttypes.h>
544	#if UINTMAX_MAX > 0xffffffffU	591	#if (defined INTPTR_MAX ? INTPTR_MAX : ULONG_MAX) > 0xffffffffU
545	#define ECB_PTRSIZE 8	592	#define ECB_PTRSIZE 8
546	#else	593	#else
547	#define ECB_PTRSIZE 4	594	#define ECB_PTRSIZE 4
548	#endif	595	#endif
549	#endif	596	#endif
550		597
		598	#define ECB_GCC_AMD64 (__amd64 || __amd64__ || __x86_64 || __x86_64__)
		599	#define ECB_MSVC_AMD64 (_M_AMD64 || _M_X64)
		600
551	/* work around x32 idiocy by defining proper macros */	601	/* work around x32 idiocy by defining proper macros */
552	#if __amd64 || __x86_64 || _M_AMD64 || _M_X64	602	#if ECB_GCC_AMD64 || ECB_MSVC_AMD64
553	#if _ILP32	603	#if _ILP32
554	#define ECB_AMD64_X32 1	604	#define ECB_AMD64_X32 1
555	#else	605	#else
556	#define ECB_AMD64 1	606	#define ECB_AMD64 1
557	#endif	607	#endif
…		…
562	* causing enormous grief in return for some better fake benchmark numbers.	612	* causing enormous grief in return for some better fake benchmark numbers.
563	* or so.	613	* or so.
564	* we try to detect these and simply assume they are not gcc - if they have	614	* we try to detect these and simply assume they are not gcc - if they have
565	* an issue with that they should have done it right in the first place.	615	* an issue with that they should have done it right in the first place.
566	*/	616	*/
567	#ifndef ECB_GCC_VERSION
568	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__	617	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__
569	#define ECB_GCC_VERSION(major,minor) 0	618	#define ECB_GCC_VERSION(major,minor) 0
570	#else	619	#else
571	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))	620	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))
572	#endif	621	#endif
		622
		623	#define ECB_CLANG_VERSION(major,minor) (__clang_major__ > (major) || (__clang_major__ == (major) && __clang_minor__ >= (minor)))
		624
		625	#if __clang__ && defined __has_builtin
		626	#define ECB_CLANG_BUILTIN(x) __has_builtin (x)
		627	#else
		628	#define ECB_CLANG_BUILTIN(x) 0
		629	#endif
		630
		631	#if __clang__ && defined __has_extension
		632	#define ECB_CLANG_EXTENSION(x) __has_extension (x)
		633	#else
		634	#define ECB_CLANG_EXTENSION(x) 0
573	#endif	635	#endif
574		636
575	#define ECB_CPP (__cplusplus+0)	637	#define ECB_CPP (__cplusplus+0)
576	#define ECB_CPP11 (__cplusplus >= 201103L)	638	#define ECB_CPP11 (__cplusplus >= 201103L)
		639	#define ECB_CPP14 (__cplusplus >= 201402L)
		640	#define ECB_CPP17 (__cplusplus >= 201703L)
577		641
578	#if ECB_CPP	642	#if ECB_CPP
579	#define ECB_C 0	643	#define ECB_C 0
580	#define ECB_STDC_VERSION 0	644	#define ECB_STDC_VERSION 0
581	#else	645	#else
…		…
583	#define ECB_STDC_VERSION __STDC_VERSION__	647	#define ECB_STDC_VERSION __STDC_VERSION__
584	#endif	648	#endif
585		649
586	#define ECB_C99 (ECB_STDC_VERSION >= 199901L)	650	#define ECB_C99 (ECB_STDC_VERSION >= 199901L)
587	#define ECB_C11 (ECB_STDC_VERSION >= 201112L)	651	#define ECB_C11 (ECB_STDC_VERSION >= 201112L)
		652	#define ECB_C17 (ECB_STDC_VERSION >= 201710L)
588		653
589	#if ECB_CPP	654	#if ECB_CPP
590	#define ECB_EXTERN_C extern "C"	655	#define ECB_EXTERN_C extern "C"
591	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {	656	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {
592	#define ECB_EXTERN_C_END }	657	#define ECB_EXTERN_C_END }
…		…
607		672
608	#if ECB_NO_SMP	673	#if ECB_NO_SMP
609	#define ECB_MEMORY_FENCE do { } while (0)	674	#define ECB_MEMORY_FENCE do { } while (0)
610	#endif	675	#endif
611		676
		677	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/compiler_ref/compiler_builtins.html */
		678	#if __xlC__ && ECB_CPP
		679	#include <builtins.h>
		680	#endif
		681
		682	#if 1400 <= _MSC_VER
		683	#include <intrin.h> /* fence functions _ReadBarrier, also bit search functions _BitScanReverse */
		684	#endif
		685
612	#ifndef ECB_MEMORY_FENCE	686	#ifndef ECB_MEMORY_FENCE
613	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	687	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
		688	#define ECB_MEMORY_FENCE_RELAXED __asm__ __volatile__ ("" : : : "memory")
614	#if __i386 || __i386__	689	#if __i386 || __i386__
615	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")	690	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")
616	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")	691	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
617	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	692	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
618	#elif __amd64 || __amd64__ || __x86_64 || __x86_64__	693	#elif ECB_GCC_AMD64
619	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")	694	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")
620	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")	695	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
621	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	696	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
622	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__	697	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__
623	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")	698	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")
		699	#elif defined __ARM_ARCH_2__ \
		700	|| defined __ARM_ARCH_3__ || defined __ARM_ARCH_3M__ \
		701	|| defined __ARM_ARCH_4__ || defined __ARM_ARCH_4T__ \
		702	|| defined __ARM_ARCH_5__ || defined __ARM_ARCH_5E__ \
		703	|| defined __ARM_ARCH_5T__ || defined __ARM_ARCH_5TE__ \
		704	|| defined __ARM_ARCH_5TEJ__
		705	/* should not need any, unless running old code on newer cpu - arm doesn't support that */
624	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \	706	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \
625	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__	707	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__ \
		708	|| defined __ARM_ARCH_6T2__
626	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")	709	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")
627	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \	710	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \
628	|| defined __ARM_ARCH_7M__ || defined __ARM_ARCH_7R__	711	|| defined __ARM_ARCH_7R__ || defined __ARM_ARCH_7M__
629	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")	712	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")
630	#elif __aarch64__	713	#elif __aarch64__
631	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb ish" : : : "memory")	714	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb ish" : : : "memory")
632	#elif (__sparc || __sparc__) && !__sparcv8	715	#elif (__sparc || __sparc__) && !(__sparc_v8__ || defined __sparcv8)
633	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")	716	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")
634	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")	717	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")
635	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")	718	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")
636	#elif defined __s390__ || defined __s390x__	719	#elif defined __s390__ || defined __s390x__
637	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")	720	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")
…		…
660	#if ECB_GCC_VERSION(4,7)	743	#if ECB_GCC_VERSION(4,7)
661	/* see comment below (stdatomic.h) about the C11 memory model. */	744	/* see comment below (stdatomic.h) about the C11 memory model. */
662	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)	745	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)
663	#define ECB_MEMORY_FENCE_ACQUIRE __atomic_thread_fence (__ATOMIC_ACQUIRE)	746	#define ECB_MEMORY_FENCE_ACQUIRE __atomic_thread_fence (__ATOMIC_ACQUIRE)
664	#define ECB_MEMORY_FENCE_RELEASE __atomic_thread_fence (__ATOMIC_RELEASE)	747	#define ECB_MEMORY_FENCE_RELEASE __atomic_thread_fence (__ATOMIC_RELEASE)
		748	#define ECB_MEMORY_FENCE_RELAXED __atomic_thread_fence (__ATOMIC_RELAXED)
665		749
666	/* The __has_feature syntax from clang is so misdesigned that we cannot use it	750	#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.	751	/* see comment below (stdatomic.h) about the C11 memory model. */
672	* #define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)	752	#define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)
673	* #define ECB_MEMORY_FENCE_ACQUIRE __c11_atomic_thread_fence (__ATOMIC_ACQUIRE)	753	#define ECB_MEMORY_FENCE_ACQUIRE __c11_atomic_thread_fence (__ATOMIC_ACQUIRE)
674	* #define ECB_MEMORY_FENCE_RELEASE __c11_atomic_thread_fence (__ATOMIC_RELEASE)	754	#define ECB_MEMORY_FENCE_RELEASE __c11_atomic_thread_fence (__ATOMIC_RELEASE)
675	*/	755	#define ECB_MEMORY_FENCE_RELAXED __c11_atomic_thread_fence (__ATOMIC_RELAXED)
676		756
677	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__	757	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__
678	#define ECB_MEMORY_FENCE __sync_synchronize ()	758	#define ECB_MEMORY_FENCE __sync_synchronize ()
679	#elif _MSC_VER >= 1500 /* VC++ 2008 */	759	#elif _MSC_VER >= 1500 /* VC++ 2008 */
680	/* apparently, microsoft broke all the memory barrier stuff in Visual Studio 2008... */	760	/* apparently, microsoft broke all the memory barrier stuff in Visual Studio 2008... */
…		…
690	#elif defined _WIN32	770	#elif defined _WIN32
691	#include <WinNT.h>	771	#include <WinNT.h>
692	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */	772	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */
693	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	773	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
694	#include <mbarrier.h>	774	#include <mbarrier.h>
695	#define ECB_MEMORY_FENCE __machine_rw_barrier ()	775	#define ECB_MEMORY_FENCE __machine_rw_barrier ()
696	#define ECB_MEMORY_FENCE_ACQUIRE __machine_r_barrier ()	776	#define ECB_MEMORY_FENCE_ACQUIRE __machine_acq_barrier ()
697	#define ECB_MEMORY_FENCE_RELEASE __machine_w_barrier ()	777	#define ECB_MEMORY_FENCE_RELEASE __machine_rel_barrier ()
		778	#define ECB_MEMORY_FENCE_RELAXED __compiler_barrier ()
698	#elif __xlC__	779	#elif __xlC__
699	#define ECB_MEMORY_FENCE __sync ()	780	#define ECB_MEMORY_FENCE __sync ()
700	#endif	781	#endif
701	#endif	782	#endif
702		783
703	#ifndef ECB_MEMORY_FENCE	784	#ifndef ECB_MEMORY_FENCE
704	#if ECB_C11 && !defined __STDC_NO_ATOMICS__	785	#if ECB_C11 && !defined __STDC_NO_ATOMICS__
705	/* we assume that these memory fences work on all variables/all memory accesses, */	786	/* we assume that these memory fences work on all variables/all memory accesses, */
706	/* not just C11 atomics and atomic accesses */	787	/* not just C11 atomics and atomic accesses */
707	#include <stdatomic.h>	788	#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)	789	#define ECB_MEMORY_FENCE atomic_thread_fence (memory_order_seq_cst)
		790	#define ECB_MEMORY_FENCE_ACQUIRE atomic_thread_fence (memory_order_acquire)
		791	#define ECB_MEMORY_FENCE_RELEASE atomic_thread_fence (memory_order_release)
717	#endif	792	#endif
718	#endif	793	#endif
719		794
720	#ifndef ECB_MEMORY_FENCE	795	#ifndef ECB_MEMORY_FENCE
721	#if !ECB_AVOID_PTHREADS	796	#if !ECB_AVOID_PTHREADS
…		…
741		816
742	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE	817	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE
743	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	818	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
744	#endif	819	#endif
745		820
		821	#if !defined ECB_MEMORY_FENCE_RELAXED && defined ECB_MEMORY_FENCE
		822	#define ECB_MEMORY_FENCE_RELAXED ECB_MEMORY_FENCE /* very heavy-handed */
		823	#endif
		824
746	/*****************************************************************************/	825	/*****************************************************************************/
747		826
748	#if __cplusplus	827	#if ECB_CPP
749	#define ecb_inline static inline	828	#define ecb_inline static inline
750	#elif ECB_GCC_VERSION(2,5)	829	#elif ECB_GCC_VERSION(2,5)
751	#define ecb_inline static __inline__	830	#define ecb_inline static __inline__
752	#elif ECB_C99	831	#elif ECB_C99
753	#define ecb_inline static inline	832	#define ecb_inline static inline
…		…
767		846
768	#define ECB_CONCAT_(a, b) a ## b	847	#define ECB_CONCAT_(a, b) a ## b
769	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)	848	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)
770	#define ECB_STRINGIFY_(a) # a	849	#define ECB_STRINGIFY_(a) # a
771	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)	850	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)
		851	#define ECB_STRINGIFY_EXPR(expr) ((expr), ECB_STRINGIFY_ (expr))
772		852
773	#define ecb_function_ ecb_inline	853	#define ecb_function_ ecb_inline
774		854
775	#if ECB_GCC_VERSION(3,1)	855	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_VERSION(2,8)
776	#define ecb_attribute(attrlist) __attribute__(attrlist)	856	#define ecb_attribute(attrlist) __attribute__ (attrlist)
		857	#else
		858	#define ecb_attribute(attrlist)
		859	#endif
		860
		861	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_constant_p)
777	#define ecb_is_constant(expr) __builtin_constant_p (expr)	862	#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	863	#else
781	#define ecb_attribute(attrlist)
782
783	/* possible C11 impl for integral types	864	/* possible C11 impl for integral types
784	typedef struct ecb_is_constant_struct ecb_is_constant_struct;	865	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)) */	866	#define ecb_is_constant(expr) _Generic ((1 ? (struct ecb_is_constant_struct *)0 : (void *)((expr) - (expr)), ecb_is_constant_struct *: 0, default: 1)) */
786		867
787	#define ecb_is_constant(expr) 0	868	#define ecb_is_constant(expr) 0
		869	#endif
		870
		871	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_expect)
		872	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))
		873	#else
788	#define ecb_expect(expr,value) (expr)	874	#define ecb_expect(expr,value) (expr)
		875	#endif
		876
		877	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_prefetch)
		878	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)
		879	#else
789	#define ecb_prefetch(addr,rw,locality)	880	#define ecb_prefetch(addr,rw,locality)
790	#endif	881	#endif
791		882
792	/* no emulation for ecb_decltype */	883	/* no emulation for ecb_decltype */
793	#if ECB_GCC_VERSION(4,5)	884	#if ECB_CPP11
		885	// older implementations might have problems with decltype(x)::type, work around it
		886	template<class T> struct ecb_decltype_t { typedef T type; };
794	#define ecb_decltype(x) __decltype(x)	887	#define ecb_decltype(x) ecb_decltype_t<decltype (x)>::type
795	#elif ECB_GCC_VERSION(3,0)	888	#elif ECB_GCC_VERSION(3,0) || ECB_CLANG_VERSION(2,8)
796	#define ecb_decltype(x) __typeof(x)	889	#define ecb_decltype(x) __typeof__ (x)
797	#endif	890	#endif
798		891
		892	#if _MSC_VER >= 1300
		893	#define ecb_deprecated __declspec (deprecated)
		894	#else
		895	#define ecb_deprecated ecb_attribute ((__deprecated__))
		896	#endif
		897
		898	#if _MSC_VER >= 1500
		899	#define ecb_deprecated_message(msg) __declspec (deprecated (msg))
		900	#elif ECB_GCC_VERSION(4,5)
		901	#define ecb_deprecated_message(msg) ecb_attribute ((__deprecated__ (msg))
		902	#else
		903	#define ecb_deprecated_message(msg) ecb_deprecated
		904	#endif
		905
		906	#if _MSC_VER >= 1400
		907	#define ecb_noinline __declspec (noinline)
		908	#else
799	#define ecb_noinline ecb_attribute ((__noinline__))	909	#define ecb_noinline ecb_attribute ((__noinline__))
		910	#endif
		911
800	#define ecb_unused ecb_attribute ((__unused__))	912	#define ecb_unused ecb_attribute ((__unused__))
801	#define ecb_const ecb_attribute ((__const__))	913	#define ecb_const ecb_attribute ((__const__))
802	#define ecb_pure ecb_attribute ((__pure__))	914	#define ecb_pure ecb_attribute ((__pure__))
803		915
804	#if ECB_C11	916	#if ECB_C11 || __IBMC_NORETURN
		917	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/language_ref/noreturn.html */
805	#define ecb_noreturn _Noreturn	918	#define ecb_noreturn _Noreturn
		919	#elif ECB_CPP11
		920	#define ecb_noreturn [[noreturn]]
		921	#elif _MSC_VER >= 1200
		922	/* http://msdn.microsoft.com/en-us/library/k6ktzx3s.aspx */
		923	#define ecb_noreturn __declspec (noreturn)
806	#else	924	#else
807	#define ecb_noreturn ecb_attribute ((__noreturn__))	925	#define ecb_noreturn ecb_attribute ((__noreturn__))
808	#endif	926	#endif
809		927
810	#if ECB_GCC_VERSION(4,3)	928	#if ECB_GCC_VERSION(4,3)
…		…
825	/* for compatibility to the rest of the world */	943	/* for compatibility to the rest of the world */
826	#define ecb_likely(expr) ecb_expect_true (expr)	944	#define ecb_likely(expr) ecb_expect_true (expr)
827	#define ecb_unlikely(expr) ecb_expect_false (expr)	945	#define ecb_unlikely(expr) ecb_expect_false (expr)
828		946
829	/* count trailing zero bits and count # of one bits */	947	/* count trailing zero bits and count # of one bits */
830	#if ECB_GCC_VERSION(3,4)	948	#if ECB_GCC_VERSION(3,4) \
		949	|| (ECB_CLANG_BUILTIN(__builtin_clz) && ECB_CLANG_BUILTIN(__builtin_clzll) \
		950	&& ECB_CLANG_BUILTIN(__builtin_ctz) && ECB_CLANG_BUILTIN(__builtin_ctzll) \
		951	&& ECB_CLANG_BUILTIN(__builtin_popcount))
831	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */	952	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */
832	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)	953	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)
833	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)	954	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)
834	#define ecb_ctz32(x) __builtin_ctz (x)	955	#define ecb_ctz32(x) __builtin_ctz (x)
835	#define ecb_ctz64(x) __builtin_ctzll (x)	956	#define ecb_ctz64(x) __builtin_ctzll (x)
836	#define ecb_popcount32(x) __builtin_popcount (x)	957	#define ecb_popcount32(x) __builtin_popcount (x)
837	/* no popcountll */	958	/* no popcountll */
838	#else	959	#else
839	ecb_function_ int ecb_ctz32 (uint32_t x) ecb_const;	960	ecb_function_ ecb_const int ecb_ctz32 (uint32_t x);
840	ecb_function_ int	961	ecb_function_ ecb_const int
841	ecb_ctz32 (uint32_t x)	962	ecb_ctz32 (uint32_t x)
842	{	963	{
		964	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		965	unsigned long r;
		966	_BitScanForward (&r, x);
		967	return (int)r;
		968	#else
843	int r = 0;	969	int r = 0;
844		970
845	x &= ~x + 1; /* this isolates the lowest bit */	971	x &= ~x + 1; /* this isolates the lowest bit */
846		972
847	#if ECB_branchless_on_i386	973	#if ECB_branchless_on_i386
…		…
857	if (x & 0xff00ff00) r += 8;	983	if (x & 0xff00ff00) r += 8;
858	if (x & 0xffff0000) r += 16;	984	if (x & 0xffff0000) r += 16;
859	#endif	985	#endif
860		986
861	return r;	987	return r;
		988	#endif
862	}	989	}
863		990
864	ecb_function_ int ecb_ctz64 (uint64_t x) ecb_const;	991	ecb_function_ ecb_const int ecb_ctz64 (uint64_t x);
865	ecb_function_ int	992	ecb_function_ ecb_const int
866	ecb_ctz64 (uint64_t x)	993	ecb_ctz64 (uint64_t x)
867	{	994	{
		995	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		996	unsigned long r;
		997	_BitScanForward64 (&r, x);
		998	return (int)r;
		999	#else
868	int shift = x & 0xffffffffU ? 0 : 32;	1000	int shift = x & 0xffffffff ? 0 : 32;
869	return ecb_ctz32 (x >> shift) + shift;	1001	return ecb_ctz32 (x >> shift) + shift;
		1002	#endif
870	}	1003	}
871		1004
872	ecb_function_ int ecb_popcount32 (uint32_t x) ecb_const;	1005	ecb_function_ ecb_const int ecb_popcount32 (uint32_t x);
873	ecb_function_ int	1006	ecb_function_ ecb_const int
874	ecb_popcount32 (uint32_t x)	1007	ecb_popcount32 (uint32_t x)
875	{	1008	{
876	x -= (x >> 1) & 0x55555555;	1009	x -= (x >> 1) & 0x55555555;
877	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);	1010	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);
878	x = ((x >> 4) + x) & 0x0f0f0f0f;	1011	x = ((x >> 4) + x) & 0x0f0f0f0f;
879	x *= 0x01010101;	1012	x *= 0x01010101;
880		1013
881	return x >> 24;	1014	return x >> 24;
882	}	1015	}
883		1016
884	ecb_function_ int ecb_ld32 (uint32_t x) ecb_const;	1017	ecb_function_ ecb_const int ecb_ld32 (uint32_t x);
885	ecb_function_ int ecb_ld32 (uint32_t x)	1018	ecb_function_ ecb_const int ecb_ld32 (uint32_t x)
886	{	1019	{
		1020	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		1021	unsigned long r;
		1022	_BitScanReverse (&r, x);
		1023	return (int)r;
		1024	#else
887	int r = 0;	1025	int r = 0;
888		1026
889	if (x >> 16) { x >>= 16; r += 16; }	1027	if (x >> 16) { x >>= 16; r += 16; }
890	if (x >> 8) { x >>= 8; r += 8; }	1028	if (x >> 8) { x >>= 8; r += 8; }
891	if (x >> 4) { x >>= 4; r += 4; }	1029	if (x >> 4) { x >>= 4; r += 4; }
892	if (x >> 2) { x >>= 2; r += 2; }	1030	if (x >> 2) { x >>= 2; r += 2; }
893	if (x >> 1) { r += 1; }	1031	if (x >> 1) { r += 1; }
894		1032
895	return r;	1033	return r;
		1034	#endif
896	}	1035	}
897		1036
898	ecb_function_ int ecb_ld64 (uint64_t x) ecb_const;	1037	ecb_function_ ecb_const int ecb_ld64 (uint64_t x);
899	ecb_function_ int ecb_ld64 (uint64_t x)	1038	ecb_function_ ecb_const int ecb_ld64 (uint64_t x)
900	{	1039	{
		1040	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1041	unsigned long r;
		1042	_BitScanReverse64 (&r, x);
		1043	return (int)r;
		1044	#else
901	int r = 0;	1045	int r = 0;
902		1046
903	if (x >> 32) { x >>= 32; r += 32; }	1047	if (x >> 32) { x >>= 32; r += 32; }
904		1048
905	return r + ecb_ld32 (x);	1049	return r + ecb_ld32 (x);
		1050	#endif
906	}	1051	}
907	#endif	1052	#endif
908		1053
909	ecb_function_ ecb_bool ecb_is_pot32 (uint32_t x) ecb_const;	1054	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)); }	1055	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;	1056	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)); }	1057	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x) { return !(x & (x - 1)); }
913		1058
914	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x) ecb_const;	1059	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x);
915	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x)	1060	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x)
916	{	1061	{
917	return ( (x * 0x0802U & 0x22110U)	1062	return ( (x * 0x0802U & 0x22110U)
918	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;	1063	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;
919	}	1064	}
920		1065
921	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x) ecb_const;	1066	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x);
922	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x)	1067	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x)
923	{	1068	{
924	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);	1069	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);
925	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);	1070	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);
926	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);	1071	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);
927	x = ( x >> 8 ) | ( x << 8);	1072	x = ( x >> 8 ) | ( x << 8);
928		1073
929	return x;	1074	return x;
930	}	1075	}
931		1076
932	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x) ecb_const;	1077	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x);
933	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x)	1078	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x)
934	{	1079	{
935	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);	1080	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);
936	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);	1081	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);
937	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);	1082	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);
938	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);	1083	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);
…		…
941	return x;	1086	return x;
942	}	1087	}
943		1088
944	/* popcount64 is only available on 64 bit cpus as gcc builtin */	1089	/* popcount64 is only available on 64 bit cpus as gcc builtin */
945	/* so for this version we are lazy */	1090	/* so for this version we are lazy */
946	ecb_function_ int ecb_popcount64 (uint64_t x) ecb_const;	1091	ecb_function_ ecb_const int ecb_popcount64 (uint64_t x);
947	ecb_function_ int	1092	ecb_function_ ecb_const int
948	ecb_popcount64 (uint64_t x)	1093	ecb_popcount64 (uint64_t x)
949	{	1094	{
950	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);	1095	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);
951	}	1096	}
952		1097
953	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) ecb_const;	1098	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count);
954	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) ecb_const;	1099	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count);
955	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) ecb_const;	1100	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count);
956	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) ecb_const;	1101	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count);
957	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) ecb_const;	1102	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count);
958	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) ecb_const;	1103	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count);
959	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) ecb_const;	1104	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count);
960	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) ecb_const;	1105	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count);
961		1106
962	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }	1107	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }
963	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }	1108	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }
964	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }	1109	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }
965	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }	1110	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }
966	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }	1111	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }
967	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }	1112	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }
968	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }	1113	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }
969	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }	1114	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }
970		1115
971	#if ECB_GCC_VERSION(4,3)	1116	#if ECB_GCC_VERSION(4,3) || (ECB_CLANG_BUILTIN(__builtin_bswap32) && ECB_CLANG_BUILTIN(__builtin_bswap64))
		1117	#if ECB_GCC_VERSION(4,8) || ECB_CLANG_BUILTIN(__builtin_bswap16)
		1118	#define ecb_bswap16(x) __builtin_bswap16 (x)
		1119	#else
972	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)	1120	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)
		1121	#endif
973	#define ecb_bswap32(x) __builtin_bswap32 (x)	1122	#define ecb_bswap32(x) __builtin_bswap32 (x)
974	#define ecb_bswap64(x) __builtin_bswap64 (x)	1123	#define ecb_bswap64(x) __builtin_bswap64 (x)
		1124	#elif _MSC_VER
		1125	#include <stdlib.h>
		1126	#define ecb_bswap16(x) ((uint16_t)_byteswap_ushort ((uint16_t)(x)))
		1127	#define ecb_bswap32(x) ((uint32_t)_byteswap_ulong ((uint32_t)(x)))
		1128	#define ecb_bswap64(x) ((uint64_t)_byteswap_uint64 ((uint64_t)(x)))
975	#else	1129	#else
976	ecb_function_ uint16_t ecb_bswap16 (uint16_t x) ecb_const;	1130	ecb_function_ ecb_const uint16_t ecb_bswap16 (uint16_t x);
977	ecb_function_ uint16_t	1131	ecb_function_ ecb_const uint16_t
978	ecb_bswap16 (uint16_t x)	1132	ecb_bswap16 (uint16_t x)
979	{	1133	{
980	return ecb_rotl16 (x, 8);	1134	return ecb_rotl16 (x, 8);
981	}	1135	}
982		1136
983	ecb_function_ uint32_t ecb_bswap32 (uint32_t x) ecb_const;	1137	ecb_function_ ecb_const uint32_t ecb_bswap32 (uint32_t x);
984	ecb_function_ uint32_t	1138	ecb_function_ ecb_const uint32_t
985	ecb_bswap32 (uint32_t x)	1139	ecb_bswap32 (uint32_t x)
986	{	1140	{
987	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);	1141	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);
988	}	1142	}
989		1143
990	ecb_function_ uint64_t ecb_bswap64 (uint64_t x) ecb_const;	1144	ecb_function_ ecb_const uint64_t ecb_bswap64 (uint64_t x);
991	ecb_function_ uint64_t	1145	ecb_function_ ecb_const uint64_t
992	ecb_bswap64 (uint64_t x)	1146	ecb_bswap64 (uint64_t x)
993	{	1147	{
994	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);	1148	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);
995	}	1149	}
996	#endif	1150	#endif
997		1151
998	#if ECB_GCC_VERSION(4,5)	1152	#if ECB_GCC_VERSION(4,5) || ECB_CLANG_BUILTIN(__builtin_unreachable)
999	#define ecb_unreachable() __builtin_unreachable ()	1153	#define ecb_unreachable() __builtin_unreachable ()
1000	#else	1154	#else
1001	/* this seems to work fine, but gcc always emits a warning for it :/ */	1155	/* this seems to work fine, but gcc always emits a warning for it :/ */
1002	ecb_inline void ecb_unreachable (void) ecb_noreturn;	1156	ecb_inline ecb_noreturn void ecb_unreachable (void);
1003	ecb_inline void ecb_unreachable (void) { }	1157	ecb_inline ecb_noreturn void ecb_unreachable (void) { }
1004	#endif	1158	#endif
1005		1159
1006	/* try to tell the compiler that some condition is definitely true */	1160	/* try to tell the compiler that some condition is definitely true */
1007	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0	1161	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0
1008		1162
1009	ecb_inline unsigned char ecb_byteorder_helper (void) ecb_const;	1163	ecb_inline ecb_const uint32_t ecb_byteorder_helper (void);
1010	ecb_inline unsigned char	1164	ecb_inline ecb_const uint32_t
1011	ecb_byteorder_helper (void)	1165	ecb_byteorder_helper (void)
1012	{	1166	{
1013	/* the union code still generates code under pressure in gcc, */	1167	/* the union code still generates code under pressure in gcc, */
1014	/* but less than using pointers, and always seems to */	1168	/* but less than using pointers, and always seems to */
1015	/* successfully return a constant. */	1169	/* successfully return a constant. */
1016	/* the reason why we have this horrible preprocessor mess */	1170	/* the reason why we have this horrible preprocessor mess */
1017	/* is to avoid it in all cases, at least on common architectures */	1171	/* is to avoid it in all cases, at least on common architectures */
1018	/* or when using a recent enough gcc version (>= 4.6) */	1172	/* 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__	1173	#if (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_LITTLE_ENDIAN__) \
		1174	|| ((__i386 || __i386__ || _M_IX86 || ECB_GCC_AMD64 || ECB_MSVC_AMD64) && !__VOS__)
		1175	#define ECB_LITTLE_ENDIAN 1
1022	return 0x44;	1176	return 0x44332211;
1023	#elif __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__	1177	#elif (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__) \
		1178	|| ((__AARCH64EB__ || __MIPSEB__ || __ARMEB__) && !__VOS__)
		1179	#define ECB_BIG_ENDIAN 1
1024	return 0x11;	1180	return 0x11223344;
1025	#else	1181	#else
1026	union	1182	union
1027	{	1183	{
		1184	uint8_t c[4];
1028	uint32_t i;	1185	uint32_t u;
1029	uint8_t c;
1030	} u = { 0x11223344 };	1186	} u = { 0x11, 0x22, 0x33, 0x44 };
1031	return u.c;	1187	return u.u;
1032	#endif	1188	#endif
1033	}	1189	}
1034		1190
1035	ecb_inline ecb_bool ecb_big_endian (void) ecb_const;	1191	ecb_inline ecb_const ecb_bool ecb_big_endian (void);
1036	ecb_inline ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11; }	1192	ecb_inline ecb_const ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11223344; }
1037	ecb_inline ecb_bool ecb_little_endian (void) ecb_const;	1193	ecb_inline ecb_const ecb_bool ecb_little_endian (void);
1038	ecb_inline ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44; }	1194	ecb_inline ecb_const ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44332211; }
1039		1195
1040	#if ECB_GCC_VERSION(3,0) || ECB_C99	1196	#if ECB_GCC_VERSION(3,0) || ECB_C99
1041	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))	1197	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))
1042	#else	1198	#else
1043	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))	1199	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))
1044	#endif	1200	#endif
1045		1201
1046	#if __cplusplus	1202	#if ECB_CPP
1047	template<typename T>	1203	template<typename T>
1048	static inline T ecb_div_rd (T val, T div)	1204	static inline T ecb_div_rd (T val, T div)
1049	{	1205	{
1050	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;	1206	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;
1051	}	1207	}
…		…
1068	}	1224	}
1069	#else	1225	#else
1070	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))	1226	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))
1071	#endif	1227	#endif
1072		1228
		1229	ecb_function_ ecb_const uint32_t ecb_binary16_to_binary32 (uint32_t x);
		1230	ecb_function_ ecb_const uint32_t
		1231	ecb_binary16_to_binary32 (uint32_t x)
		1232	{
		1233	unsigned int s = (x & 0x8000) << (31 - 15);
		1234	int e = (x >> 10) & 0x001f;
		1235	unsigned int m = x & 0x03ff;
		1236
		1237	if (ecb_expect_false (e == 31))
		1238	/* infinity or NaN */
		1239	e = 255 - (127 - 15);
		1240	else if (ecb_expect_false (!e))
		1241	{
		1242	if (ecb_expect_true (!m))
		1243	/* zero, handled by code below by forcing e to 0 */
		1244	e = 0 - (127 - 15);
		1245	else
		1246	{
		1247	/* subnormal, renormalise */
		1248	unsigned int s = 10 - ecb_ld32 (m);
		1249
		1250	m = (m << s) & 0x3ff; /* mask implicit bit */
		1251	e -= s - 1;
		1252	}
		1253	}
		1254
		1255	/* e and m now are normalised, or zero, (or inf or nan) */
		1256	e += 127 - 15;
		1257
		1258	return s | (e << 23) | (m << (23 - 10));
		1259	}
		1260
		1261	ecb_function_ ecb_const uint16_t ecb_binary32_to_binary16 (uint32_t x);
		1262	ecb_function_ ecb_const uint16_t
		1263	ecb_binary32_to_binary16 (uint32_t x)
		1264	{
		1265	unsigned int s = (x >> 16) & 0x00008000; /* sign bit, the easy part */
		1266	unsigned int e = ((x >> 23) & 0x000000ff) - (127 - 15); /* the desired exponent */
		1267	unsigned int m = x & 0x007fffff;
		1268
		1269	x &= 0x7fffffff;
		1270
		1271	/* if it's within range of binary16 normals, use fast path */
		1272	if (ecb_expect_true (0x38800000 <= x && x <= 0x477fefff))
		1273	{
		1274	/* mantissa round-to-even */
		1275	m += 0x00000fff + ((m >> (23 - 10)) & 1);
		1276
		1277	/* handle overflow */
		1278	if (ecb_expect_false (m >= 0x00800000))
		1279	{
		1280	m >>= 1;
		1281	e += 1;
		1282	}
		1283
		1284	return s | (e << 10) | (m >> (23 - 10));
		1285	}
		1286
		1287	/* handle large numbers and infinity */
		1288	if (ecb_expect_true (0x477fefff < x && x <= 0x7f800000))
		1289	return s | 0x7c00;
		1290
		1291	/* handle zero, subnormals and small numbers */
		1292	if (ecb_expect_true (x < 0x38800000))
		1293	{
		1294	/* zero */
		1295	if (ecb_expect_true (!x))
		1296	return s;
		1297
		1298	/* handle subnormals */
		1299
		1300	/* too small, will be zero */
		1301	if (e < (14 - 24)) /* might not be sharp, but is good enough */
		1302	return s;
		1303
		1304	m |= 0x00800000; /* make implicit bit explicit */
		1305
		1306	/* very tricky - we need to round to the nearest e (+10) bit value */
		1307	{
		1308	unsigned int bits = 14 - e;
		1309	unsigned int half = (1 << (bits - 1)) - 1;
		1310	unsigned int even = (m >> bits) & 1;
		1311
		1312	/* if this overflows, we will end up with a normalised number */
		1313	m = (m + half + even) >> bits;
		1314	}
		1315
		1316	return s | m;
		1317	}
		1318
		1319	/* handle NaNs, preserve leftmost nan bits, but make sure we don't turn them into infinities */
		1320	m >>= 13;
		1321
		1322	return s | 0x7c00 | m | !m;
		1323	}
		1324
1073	/*******************************************************************************/	1325	/*******************************************************************************/
1074	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */	1326	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */
1075		1327
1076	/* basically, everything uses "ieee pure-endian" floating point numbers */	1328	/* basically, everything uses "ieee pure-endian" floating point numbers */
1077	/* the only noteworthy exception is ancient armle, which uses order 43218765 */	1329	/* the only noteworthy exception is ancient armle, which uses order 43218765 */
1078	#if 0 \	1330	#if 0 \
1079	|| __i386 || __i386__ \	1331	|| __i386 || __i386__ \
1080	|| __amd64 || __amd64__ || __x86_64 || __x86_64__ \	1332	|| ECB_GCC_AMD64 \
1081	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \	1333	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \
1082	|| defined __s390__ || defined __s390x__ \	1334	|| defined __s390__ || defined __s390x__ \
1083	|| defined __mips__ \	1335	|| defined __mips__ \
1084	|| defined __alpha__ \	1336	|| defined __alpha__ \
1085	|| defined __hppa__ \	1337	|| defined __hppa__ \
1086	|| defined __ia64__ \	1338	|| defined __ia64__ \
1087	|| defined __m68k__ \	1339	|| defined __m68k__ \
1088	|| defined __m88k__ \	1340	|| defined __m88k__ \
1089	|| defined __sh__ \	1341	|| defined __sh__ \
1090	|| defined _M_IX86 || defined _M_AMD64 || defined _M_IA64 \	1342	|| defined _M_IX86 || defined ECB_MSVC_AMD64 || defined _M_IA64 \
1091	|| (defined __arm__ && (defined __ARM_EABI__ || defined __EABI__ || defined __VFP_FP__ || defined _WIN32_WCE || defined __ANDROID__)) \	1343	|| (defined __arm__ && (defined __ARM_EABI__ || defined __EABI__ || defined __VFP_FP__ || defined _WIN32_WCE || defined __ANDROID__)) \
1092	|| defined __aarch64__	1344	|| defined __aarch64__
1093	#define ECB_STDFP 1	1345	#define ECB_STDFP 1
1094	#include <string.h> /* for memcpy */	1346	#include <string.h> /* for memcpy */
1095	#else	1347	#else
…		…
1111	#define ECB_NAN NAN	1363	#define ECB_NAN NAN
1112	#else	1364	#else
1113	#define ECB_NAN ECB_INFINITY	1365	#define ECB_NAN ECB_INFINITY
1114	#endif	1366	#endif
1115		1367
1116	/* converts an ieee half/binary16 to a float */	1368	#if ECB_C99 || _XOPEN_VERSION >= 600 || _POSIX_VERSION >= 200112L
1117	ecb_function_ float ecb_binary16_to_float (uint16_t x) ecb_const;	1369	#define ecb_ldexpf(x,e) ldexpf ((x), (e))
1118	ecb_function_ float	1370	#define ecb_frexpf(x,e) frexpf ((x), (e))
1119	ecb_binary16_to_float (uint16_t x)	1371	#else
1120	{	1372	#define ecb_ldexpf(x,e) (float) ldexp ((double) (x), (e))
1121	int e = (x >> 10) & 0x1f;	1373	#define ecb_frexpf(x,e) (float) frexp ((double) (x), (e))
1122	int m = x & 0x3ff;	1374	#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		1375
1133	/* convert a float to ieee single/binary32 */	1376	/* convert a float to ieee single/binary32 */
1134	ecb_function_ uint32_t ecb_float_to_binary32 (float x) ecb_const;	1377	ecb_function_ ecb_const uint32_t ecb_float_to_binary32 (float x);
1135	ecb_function_ uint32_t	1378	ecb_function_ ecb_const uint32_t
1136	ecb_float_to_binary32 (float x)	1379	ecb_float_to_binary32 (float x)
1137	{	1380	{
1138	uint32_t r;	1381	uint32_t r;
1139		1382
1140	#if ECB_STDFP	1383	#if ECB_STDFP
…		…
1147	if (x == 0e0f ) return 0x00000000U;	1390	if (x == 0e0f ) return 0x00000000U;
1148	if (x > +3.40282346638528860e+38f) return 0x7f800000U;	1391	if (x > +3.40282346638528860e+38f) return 0x7f800000U;
1149	if (x < -3.40282346638528860e+38f) return 0xff800000U;	1392	if (x < -3.40282346638528860e+38f) return 0xff800000U;
1150	if (x != x ) return 0x7fbfffffU;	1393	if (x != x ) return 0x7fbfffffU;
1151		1394
1152	m = frexpf (x, &e) * 0x1000000U;	1395	m = ecb_frexpf (x, &e) * 0x1000000U;
1153		1396
1154	r = m & 0x80000000U;	1397	r = m & 0x80000000U;
1155		1398
1156	if (r)	1399	if (r)
1157	m = -m;	1400	m = -m;
…		…
1169		1412
1170	return r;	1413	return r;
1171	}	1414	}
1172		1415
1173	/* converts an ieee single/binary32 to a float */	1416	/* converts an ieee single/binary32 to a float */
1174	ecb_function_ float ecb_binary32_to_float (uint32_t x) ecb_const;	1417	ecb_function_ ecb_const float ecb_binary32_to_float (uint32_t x);
1175	ecb_function_ float	1418	ecb_function_ ecb_const float
1176	ecb_binary32_to_float (uint32_t x)	1419	ecb_binary32_to_float (uint32_t x)
1177	{	1420	{
1178	float r;	1421	float r;
1179		1422
1180	#if ECB_STDFP	1423	#if ECB_STDFP
…		…
1190	x |= 0x800000U;	1433	x |= 0x800000U;
1191	else	1434	else
1192	e = 1;	1435	e = 1;
1193		1436
1194	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */	1437	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */
1195	r = ldexpf (x * (0.5f / 0x800000U), e - 126);	1438	r = ecb_ldexpf (x * (0.5f / 0x800000U), e - 126);
1196		1439
1197	r = neg ? -r : r;	1440	r = neg ? -r : r;
1198	#endif	1441	#endif
1199		1442
1200	return r;	1443	return r;
1201	}	1444	}
1202		1445
1203	/* convert a double to ieee double/binary64 */	1446	/* convert a double to ieee double/binary64 */
1204	ecb_function_ uint64_t ecb_double_to_binary64 (double x) ecb_const;	1447	ecb_function_ ecb_const uint64_t ecb_double_to_binary64 (double x);
1205	ecb_function_ uint64_t	1448	ecb_function_ ecb_const uint64_t
1206	ecb_double_to_binary64 (double x)	1449	ecb_double_to_binary64 (double x)
1207	{	1450	{
1208	uint64_t r;	1451	uint64_t r;
1209		1452
1210	#if ECB_STDFP	1453	#if ECB_STDFP
…		…
1239		1482
1240	return r;	1483	return r;
1241	}	1484	}
1242		1485
1243	/* converts an ieee double/binary64 to a double */	1486	/* converts an ieee double/binary64 to a double */
1244	ecb_function_ double ecb_binary64_to_double (uint64_t x) ecb_const;	1487	ecb_function_ ecb_const double ecb_binary64_to_double (uint64_t x);
1245	ecb_function_ double	1488	ecb_function_ ecb_const double
1246	ecb_binary64_to_double (uint64_t x)	1489	ecb_binary64_to_double (uint64_t x)
1247	{	1490	{
1248	double r;	1491	double r;
1249		1492
1250	#if ECB_STDFP	1493	#if ECB_STDFP
…		…
1266		1509
1267	r = neg ? -r : r;	1510	r = neg ? -r : r;
1268	#endif	1511	#endif
1269		1512
1270	return r;	1513	return r;
		1514	}
		1515
		1516	/* convert a float to ieee half/binary16 */
		1517	ecb_function_ ecb_const uint16_t ecb_float_to_binary16 (float x);
		1518	ecb_function_ ecb_const uint16_t
		1519	ecb_float_to_binary16 (float x)
		1520	{
		1521	return ecb_binary32_to_binary16 (ecb_float_to_binary32 (x));
		1522	}
		1523
		1524	/* convert an ieee half/binary16 to float */
		1525	ecb_function_ ecb_const float ecb_binary16_to_float (uint16_t x);
		1526	ecb_function_ ecb_const float
		1527	ecb_binary16_to_float (uint16_t x)
		1528	{
		1529	return ecb_binary32_to_float (ecb_binary16_to_binary32 (x));
1271	}	1530	}
1272		1531
1273	#endif	1532	#endif
1274		1533
1275	#endif	1534	#endif
…		…
1300	#define inline_size ecb_inline	1559	#define inline_size ecb_inline
1301		1560
1302	#if EV_FEATURE_CODE	1561	#if EV_FEATURE_CODE
1303	# define inline_speed ecb_inline	1562	# define inline_speed ecb_inline
1304	#else	1563	#else
1305	# define inline_speed static noinline	1564	# define inline_speed noinline static
1306	#endif	1565	#endif
1307		1566
1308	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)	1567	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)
1309		1568
1310	#if EV_MINPRI == EV_MAXPRI	1569	#if EV_MINPRI == EV_MAXPRI
1311	# define ABSPRI(w) (((W)w), 0)	1570	# define ABSPRI(w) (((W)w), 0)
1312	#else	1571	#else
1313	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)	1572	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)
1314	#endif	1573	#endif
1315		1574
1316	#define EMPTY /* required for microsofts broken pseudo-c compiler */	1575	#define EMPTY /* required for microsofts broken pseudo-c compiler */
1317	#define EMPTY2(a,b) /* used to suppress some warnings */
1318		1576
1319	typedef ev_watcher *W;	1577	typedef ev_watcher *W;
1320	typedef ev_watcher_list *WL;	1578	typedef ev_watcher_list *WL;
1321	typedef ev_watcher_time *WT;	1579	typedef ev_watcher_time *WT;
1322		1580
…		…
1347	# include "ev_win32.c"	1605	# include "ev_win32.c"
1348	#endif	1606	#endif
1349		1607
1350	/*****************************************************************************/	1608	/*****************************************************************************/
1351		1609
		1610	#if EV_USE_LINUXAIO
		1611	# include <linux/aio_abi.h> /* probably only needed for aio_context_t */
		1612	#endif
		1613
1352	/* define a suitable floor function (only used by periodics atm) */	1614	/* define a suitable floor function (only used by periodics atm) */
1353		1615
1354	#if EV_USE_FLOOR	1616	#if EV_USE_FLOOR
1355	# include <math.h>	1617	# include <math.h>
1356	# define ev_floor(v) floor (v)	1618	# define ev_floor(v) floor (v)
1357	#else	1619	#else
1358		1620
1359	#include <float.h>	1621	#include <float.h>
1360		1622
1361	/* a floor() replacement function, should be independent of ev_tstamp type */	1623	/* a floor() replacement function, should be independent of ev_tstamp type */
		1624	noinline
1362	static ev_tstamp noinline	1625	static ev_tstamp
1363	ev_floor (ev_tstamp v)	1626	ev_floor (ev_tstamp v)
1364	{	1627	{
1365	/* the choice of shift factor is not terribly important */	1628	/* the choice of shift factor is not terribly important */
1366	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */	1629	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */
1367	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;	1630	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;
…		…
1399		1662
1400	#ifdef __linux	1663	#ifdef __linux
1401	# include <sys/utsname.h>	1664	# include <sys/utsname.h>
1402	#endif	1665	#endif
1403		1666
1404	static unsigned int noinline ecb_cold	1667	noinline ecb_cold
		1668	static unsigned int
1405	ev_linux_version (void)	1669	ev_linux_version (void)
1406	{	1670	{
1407	#ifdef __linux	1671	#ifdef __linux
1408	unsigned int v = 0;	1672	unsigned int v = 0;
1409	struct utsname buf;	1673	struct utsname buf;
…		…
1438	}	1702	}
1439		1703
1440	/*****************************************************************************/	1704	/*****************************************************************************/
1441		1705
1442	#if EV_AVOID_STDIO	1706	#if EV_AVOID_STDIO
1443	static void noinline ecb_cold	1707	noinline ecb_cold
		1708	static void
1444	ev_printerr (const char *msg)	1709	ev_printerr (const char *msg)
1445	{	1710	{
1446	write (STDERR_FILENO, msg, strlen (msg));	1711	write (STDERR_FILENO, msg, strlen (msg));
1447	}	1712	}
1448	#endif	1713	#endif
1449		1714
1450	static void (*syserr_cb)(const char *msg) EV_THROW;	1715	static void (*syserr_cb)(const char *msg) EV_NOEXCEPT;
1451		1716
1452	void ecb_cold	1717	ecb_cold
		1718	void
1453	ev_set_syserr_cb (void (*cb)(const char *msg) EV_THROW) EV_THROW	1719	ev_set_syserr_cb (void (*cb)(const char *msg) EV_NOEXCEPT) EV_NOEXCEPT
1454	{	1720	{
1455	syserr_cb = cb;	1721	syserr_cb = cb;
1456	}	1722	}
1457		1723
1458	static void noinline ecb_cold	1724	noinline ecb_cold
		1725	static void
1459	ev_syserr (const char *msg)	1726	ev_syserr (const char *msg)
1460	{	1727	{
1461	if (!msg)	1728	if (!msg)
1462	msg = "(libev) system error";	1729	msg = "(libev) system error";
1463		1730
…		…
1476	abort ();	1743	abort ();
1477	}	1744	}
1478	}	1745	}
1479		1746
1480	static void *	1747	static void *
1481	ev_realloc_emul (void *ptr, long size) EV_THROW	1748	ev_realloc_emul (void *ptr, long size) EV_NOEXCEPT
1482	{	1749	{
1483	/* some systems, notably openbsd and darwin, fail to properly	1750	/* some systems, notably openbsd and darwin, fail to properly
1484	* implement realloc (x, 0) (as required by both ansi c-89 and	1751	* implement realloc (x, 0) (as required by both ansi c-89 and
1485	* the single unix specification, so work around them here.	1752	* the single unix specification, so work around them here.
1486	* recently, also (at least) fedora and debian started breaking it,	1753	* recently, also (at least) fedora and debian started breaking it,
…		…
1492		1759
1493	free (ptr);	1760	free (ptr);
1494	return 0;	1761	return 0;
1495	}	1762	}
1496		1763
1497	static void *(*alloc)(void *ptr, long size) EV_THROW = ev_realloc_emul;	1764	static void *(*alloc)(void *ptr, long size) EV_NOEXCEPT = ev_realloc_emul;
1498		1765
1499	void ecb_cold	1766	ecb_cold
		1767	void
1500	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_THROW) EV_THROW	1768	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_NOEXCEPT) EV_NOEXCEPT
1501	{	1769	{
1502	alloc = cb;	1770	alloc = cb;
1503	}	1771	}
1504		1772
1505	inline_speed void *	1773	inline_speed void *
…		…
1532	typedef struct	1800	typedef struct
1533	{	1801	{
1534	WL head;	1802	WL head;
1535	unsigned char events; /* the events watched for */	1803	unsigned char events; /* the events watched for */
1536	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */	1804	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */
1537	unsigned char emask; /* the epoll backend stores the actual kernel mask in here */	1805	unsigned char emask; /* some backends store the actual kernel mask in here */
1538	unsigned char unused;	1806	unsigned char unused;
1539	#if EV_USE_EPOLL	1807	#if EV_USE_EPOLL
1540	unsigned int egen; /* generation counter to counter epoll bugs */	1808	unsigned int egen; /* generation counter to counter epoll bugs */
1541	#endif	1809	#endif
1542	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP	1810	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP
…		…
1622		1890
1623	/*****************************************************************************/	1891	/*****************************************************************************/
1624		1892
1625	#ifndef EV_HAVE_EV_TIME	1893	#ifndef EV_HAVE_EV_TIME
1626	ev_tstamp	1894	ev_tstamp
1627	ev_time (void) EV_THROW	1895	ev_time (void) EV_NOEXCEPT
1628	{	1896	{
1629	#if EV_USE_REALTIME	1897	#if EV_USE_REALTIME
1630	if (expect_true (have_realtime))	1898	if (expect_true (have_realtime))
1631	{	1899	{
1632	struct timespec ts;	1900	struct timespec ts;
…		…
1656	return ev_time ();	1924	return ev_time ();
1657	}	1925	}
1658		1926
1659	#if EV_MULTIPLICITY	1927	#if EV_MULTIPLICITY
1660	ev_tstamp	1928	ev_tstamp
1661	ev_now (EV_P) EV_THROW	1929	ev_now (EV_P) EV_NOEXCEPT
1662	{	1930	{
1663	return ev_rt_now;	1931	return ev_rt_now;
1664	}	1932	}
1665	#endif	1933	#endif
1666		1934
1667	void	1935	void
1668	ev_sleep (ev_tstamp delay) EV_THROW	1936	ev_sleep (ev_tstamp delay) EV_NOEXCEPT
1669	{	1937	{
1670	if (delay > 0.)	1938	if (delay > 0.)
1671	{	1939	{
1672	#if EV_USE_NANOSLEEP	1940	#if EV_USE_NANOSLEEP
1673	struct timespec ts;	1941	struct timespec ts;
1674		1942
1675	EV_TS_SET (ts, delay);	1943	EV_TS_SET (ts, delay);
1676	nanosleep (&ts, 0);	1944	nanosleep (&ts, 0);
1677	#elif defined _WIN32	1945	#elif defined _WIN32
		1946	/* maybe this should round up, as ms is very low resolution */
		1947	/* compared to select (µs) or nanosleep (ns) */
1678	Sleep ((unsigned long)(delay * 1e3));	1948	Sleep ((unsigned long)(delay * 1e3));
1679	#else	1949	#else
1680	struct timeval tv;	1950	struct timeval tv;
1681		1951
1682	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */	1952	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */
…		…
1713	}	1983	}
1714		1984
1715	return ncur;	1985	return ncur;
1716	}	1986	}
1717		1987
1718	static void * noinline ecb_cold	1988	noinline ecb_cold
		1989	static void *
1719	array_realloc (int elem, void *base, int *cur, int cnt)	1990	array_realloc (int elem, void *base, int *cur, int cnt)
1720	{	1991	{
1721	*cur = array_nextsize (elem, *cur, cnt);	1992	*cur = array_nextsize (elem, *cur, cnt);
1722	return ev_realloc (base, elem * *cur);	1993	return ev_realloc (base, elem * *cur);
1723	}	1994	}
1724		1995
		1996	#define array_needsize_noinit(base,offset,count)
		1997
1725	#define array_init_zero(base,count) \	1998	#define array_needsize_zerofill(base,offset,count) \
1726	memset ((void *)(base), 0, sizeof (*(base)) * (count))	1999	memset ((void *)(base + offset), 0, sizeof (*(base)) * (count))
1727		2000
1728	#define array_needsize(type,base,cur,cnt,init) \	2001	#define array_needsize(type,base,cur,cnt,init) \
1729	if (expect_false ((cnt) > (cur))) \	2002	if (expect_false ((cnt) > (cur))) \
1730	{ \	2003	{ \
1731	int ecb_unused ocur_ = (cur); \	2004	ecb_unused int ocur_ = (cur); \
1732	(base) = (type *)array_realloc \	2005	(base) = (type *)array_realloc \
1733	(sizeof (type), (base), &(cur), (cnt)); \	2006	(sizeof (type), (base), &(cur), (cnt)); \
1734	init ((base) + (ocur_), (cur) - ocur_); \	2007	init ((base), ocur_, ((cur) - ocur_)); \
1735	}	2008	}
1736		2009
1737	#if 0	2010	#if 0
1738	#define array_slim(type,stem) \	2011	#define array_slim(type,stem) \
1739	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \	2012	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	2021	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0
1749		2022
1750	/*****************************************************************************/	2023	/*****************************************************************************/
1751		2024
1752	/* dummy callback for pending events */	2025	/* dummy callback for pending events */
1753	static void noinline	2026	noinline
		2027	static void
1754	pendingcb (EV_P_ ev_prepare *w, int revents)	2028	pendingcb (EV_P_ ev_prepare *w, int revents)
1755	{	2029	{
1756	}	2030	}
1757		2031
1758	void noinline	2032	noinline
		2033	void
1759	ev_feed_event (EV_P_ void *w, int revents) EV_THROW	2034	ev_feed_event (EV_P_ void *w, int revents) EV_NOEXCEPT
1760	{	2035	{
1761	W w_ = (W)w;	2036	W w_ = (W)w;
1762	int pri = ABSPRI (w_);	2037	int pri = ABSPRI (w_);
1763		2038
1764	if (expect_false (w_->pending))	2039	if (expect_false (w_->pending))
1765	pendings [pri][w_->pending - 1].events |= revents;	2040	pendings [pri][w_->pending - 1].events |= revents;
1766	else	2041	else
1767	{	2042	{
1768	w_->pending = ++pendingcnt [pri];	2043	w_->pending = ++pendingcnt [pri];
1769	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, EMPTY2);	2044	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, array_needsize_noinit);
1770	pendings [pri][w_->pending - 1].w = w_;	2045	pendings [pri][w_->pending - 1].w = w_;
1771	pendings [pri][w_->pending - 1].events = revents;	2046	pendings [pri][w_->pending - 1].events = revents;
1772	}	2047	}
1773		2048
1774	pendingpri = NUMPRI - 1;	2049	pendingpri = NUMPRI - 1;
1775	}	2050	}
1776		2051
1777	inline_speed void	2052	inline_speed void
1778	feed_reverse (EV_P_ W w)	2053	feed_reverse (EV_P_ W w)
1779	{	2054	{
1780	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, EMPTY2);	2055	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, array_needsize_noinit);
1781	rfeeds [rfeedcnt++] = w;	2056	rfeeds [rfeedcnt++] = w;
1782	}	2057	}
1783		2058
1784	inline_size void	2059	inline_size void
1785	feed_reverse_done (EV_P_ int revents)	2060	feed_reverse_done (EV_P_ int revents)
…		…
1825	if (expect_true (!anfd->reify))	2100	if (expect_true (!anfd->reify))
1826	fd_event_nocheck (EV_A_ fd, revents);	2101	fd_event_nocheck (EV_A_ fd, revents);
1827	}	2102	}
1828		2103
1829	void	2104	void
1830	ev_feed_fd_event (EV_P_ int fd, int revents) EV_THROW	2105	ev_feed_fd_event (EV_P_ int fd, int revents) EV_NOEXCEPT
1831	{	2106	{
1832	if (fd >= 0 && fd < anfdmax)	2107	if (fd >= 0 && fd < anfdmax)
1833	fd_event_nocheck (EV_A_ fd, revents);	2108	fd_event_nocheck (EV_A_ fd, revents);
1834	}	2109	}
1835		2110
…		…
1893		2168
1894	fdchangecnt = 0;	2169	fdchangecnt = 0;
1895	}	2170	}
1896		2171
1897	/* something about the given fd changed */	2172	/* something about the given fd changed */
1898	inline_size void	2173	inline_size
		2174	void
1899	fd_change (EV_P_ int fd, int flags)	2175	fd_change (EV_P_ int fd, int flags)
1900	{	2176	{
1901	unsigned char reify = anfds [fd].reify;	2177	unsigned char reify = anfds [fd].reify;
1902	anfds [fd].reify |= flags;	2178	anfds [fd].reify |= flags;
1903		2179
1904	if (expect_true (!reify))	2180	if (expect_true (!reify))
1905	{	2181	{
1906	++fdchangecnt;	2182	++fdchangecnt;
1907	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, EMPTY2);	2183	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, array_needsize_noinit);
1908	fdchanges [fdchangecnt - 1] = fd;	2184	fdchanges [fdchangecnt - 1] = fd;
1909	}	2185	}
1910	}	2186	}
1911		2187
1912	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */	2188	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */
1913	inline_speed void ecb_cold	2189	inline_speed ecb_cold void
1914	fd_kill (EV_P_ int fd)	2190	fd_kill (EV_P_ int fd)
1915	{	2191	{
1916	ev_io *w;	2192	ev_io *w;
1917		2193
1918	while ((w = (ev_io *)anfds [fd].head))	2194	while ((w = (ev_io *)anfds [fd].head))
…		…
1921	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);	2197	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);
1922	}	2198	}
1923	}	2199	}
1924		2200
1925	/* check whether the given fd is actually valid, for error recovery */	2201	/* check whether the given fd is actually valid, for error recovery */
1926	inline_size int ecb_cold	2202	inline_size ecb_cold int
1927	fd_valid (int fd)	2203	fd_valid (int fd)
1928	{	2204	{
1929	#ifdef _WIN32	2205	#ifdef _WIN32
1930	return EV_FD_TO_WIN32_HANDLE (fd) != -1;	2206	return EV_FD_TO_WIN32_HANDLE (fd) != -1;
1931	#else	2207	#else
1932	return fcntl (fd, F_GETFD) != -1;	2208	return fcntl (fd, F_GETFD) != -1;
1933	#endif	2209	#endif
1934	}	2210	}
1935		2211
1936	/* called on EBADF to verify fds */	2212	/* called on EBADF to verify fds */
1937	static void noinline ecb_cold	2213	noinline ecb_cold
		2214	static void
1938	fd_ebadf (EV_P)	2215	fd_ebadf (EV_P)
1939	{	2216	{
1940	int fd;	2217	int fd;
1941		2218
1942	for (fd = 0; fd < anfdmax; ++fd)	2219	for (fd = 0; fd < anfdmax; ++fd)
…		…
1944	if (!fd_valid (fd) && errno == EBADF)	2221	if (!fd_valid (fd) && errno == EBADF)
1945	fd_kill (EV_A_ fd);	2222	fd_kill (EV_A_ fd);
1946	}	2223	}
1947		2224
1948	/* called on ENOMEM in select/poll to kill some fds and retry */	2225	/* called on ENOMEM in select/poll to kill some fds and retry */
1949	static void noinline ecb_cold	2226	noinline ecb_cold
		2227	static void
1950	fd_enomem (EV_P)	2228	fd_enomem (EV_P)
1951	{	2229	{
1952	int fd;	2230	int fd;
1953		2231
1954	for (fd = anfdmax; fd--; )	2232	for (fd = anfdmax; fd--; )
…		…
1958	break;	2236	break;
1959	}	2237	}
1960	}	2238	}
1961		2239
1962	/* usually called after fork if backend needs to re-arm all fds from scratch */	2240	/* usually called after fork if backend needs to re-arm all fds from scratch */
1963	static void noinline	2241	noinline
		2242	static void
1964	fd_rearm_all (EV_P)	2243	fd_rearm_all (EV_P)
1965	{	2244	{
1966	int fd;	2245	int fd;
1967		2246
1968	for (fd = 0; fd < anfdmax; ++fd)	2247	for (fd = 0; fd < anfdmax; ++fd)
…		…
2149		2428
2150	/*****************************************************************************/	2429	/*****************************************************************************/
2151		2430
2152	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	2431	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2153		2432
2154	static void noinline ecb_cold	2433	noinline ecb_cold
		2434	static void
2155	evpipe_init (EV_P)	2435	evpipe_init (EV_P)
2156	{	2436	{
2157	if (!ev_is_active (&pipe_w))	2437	if (!ev_is_active (&pipe_w))
2158	{	2438	{
2159	int fds [2];	2439	int fds [2];
…		…
2230	#endif	2510	#endif
2231	{	2511	{
2232	#ifdef _WIN32	2512	#ifdef _WIN32
2233	WSABUF buf;	2513	WSABUF buf;
2234	DWORD sent;	2514	DWORD sent;
2235	buf.buf = &buf;	2515	buf.buf = (char *)&buf;
2236	buf.len = 1;	2516	buf.len = 1;
2237	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);	2517	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);
2238	#else	2518	#else
2239	write (evpipe [1], &(evpipe [1]), 1);	2519	write (evpipe [1], &(evpipe [1]), 1);
2240	#endif	2520	#endif
…		…
2312	}	2592	}
2313		2593
2314	/*****************************************************************************/	2594	/*****************************************************************************/
2315		2595
2316	void	2596	void
2317	ev_feed_signal (int signum) EV_THROW	2597	ev_feed_signal (int signum) EV_NOEXCEPT
2318	{	2598	{
2319	#if EV_MULTIPLICITY	2599	#if EV_MULTIPLICITY
2320	EV_P;	2600	EV_P;
2321	ECB_MEMORY_FENCE_ACQUIRE;	2601	ECB_MEMORY_FENCE_ACQUIRE;
2322	EV_A = signals [signum - 1].loop;	2602	EV_A = signals [signum - 1].loop;
…		…
2337	#endif	2617	#endif
2338		2618
2339	ev_feed_signal (signum);	2619	ev_feed_signal (signum);
2340	}	2620	}
2341		2621
2342	void noinline	2622	noinline
		2623	void
2343	ev_feed_signal_event (EV_P_ int signum) EV_THROW	2624	ev_feed_signal_event (EV_P_ int signum) EV_NOEXCEPT
2344	{	2625	{
2345	WL w;	2626	WL w;
2346		2627
2347	if (expect_false (signum <= 0 || signum >= EV_NSIG))	2628	if (expect_false (signum <= 0 || signum >= EV_NSIG))
2348	return;	2629	return;
…		…
2457	# include "ev_kqueue.c"	2738	# include "ev_kqueue.c"
2458	#endif	2739	#endif
2459	#if EV_USE_EPOLL	2740	#if EV_USE_EPOLL
2460	# include "ev_epoll.c"	2741	# include "ev_epoll.c"
2461	#endif	2742	#endif
		2743	#if EV_USE_LINUXAIO
		2744	# include "ev_linuxaio.c"
		2745	#endif
2462	#if EV_USE_POLL	2746	#if EV_USE_POLL
2463	# include "ev_poll.c"	2747	# include "ev_poll.c"
2464	#endif	2748	#endif
2465	#if EV_USE_SELECT	2749	#if EV_USE_SELECT
2466	# include "ev_select.c"	2750	# include "ev_select.c"
2467	#endif	2751	#endif
2468		2752
2469	int ecb_cold	2753	ecb_cold int
2470	ev_version_major (void) EV_THROW	2754	ev_version_major (void) EV_NOEXCEPT
2471	{	2755	{
2472	return EV_VERSION_MAJOR;	2756	return EV_VERSION_MAJOR;
2473	}	2757	}
2474		2758
2475	int ecb_cold	2759	ecb_cold int
2476	ev_version_minor (void) EV_THROW	2760	ev_version_minor (void) EV_NOEXCEPT
2477	{	2761	{
2478	return EV_VERSION_MINOR;	2762	return EV_VERSION_MINOR;
2479	}	2763	}
2480		2764
2481	/* return true if we are running with elevated privileges and should ignore env variables */	2765	/* return true if we are running with elevated privileges and should ignore env variables */
2482	int inline_size ecb_cold	2766	inline_size ecb_cold int
2483	enable_secure (void)	2767	enable_secure (void)
2484	{	2768	{
2485	#ifdef _WIN32	2769	#ifdef _WIN32
2486	return 0;	2770	return 0;
2487	#else	2771	#else
2488	return getuid () != geteuid ()	2772	return getuid () != geteuid ()
2489	|| getgid () != getegid ();	2773	|| getgid () != getegid ();
2490	#endif	2774	#endif
2491	}	2775	}
2492		2776
2493	unsigned int ecb_cold	2777	ecb_cold
		2778	unsigned int
2494	ev_supported_backends (void) EV_THROW	2779	ev_supported_backends (void) EV_NOEXCEPT
2495	{	2780	{
2496	unsigned int flags = 0;	2781	unsigned int flags = 0;
2497		2782
2498	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;	2783	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;
2499	if (EV_USE_KQUEUE) flags |= EVBACKEND_KQUEUE;	2784	if (EV_USE_KQUEUE ) flags |= EVBACKEND_KQUEUE;
2500	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;	2785	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;
		2786	if (EV_USE_LINUXAIO) flags |= EVBACKEND_LINUXAIO;
2501	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;	2787	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;
2502	if (EV_USE_SELECT) flags |= EVBACKEND_SELECT;	2788	if (EV_USE_SELECT ) flags |= EVBACKEND_SELECT;
2503		2789
2504	return flags;	2790	return flags;
2505	}	2791	}
2506		2792
2507	unsigned int ecb_cold	2793	ecb_cold
		2794	unsigned int
2508	ev_recommended_backends (void) EV_THROW	2795	ev_recommended_backends (void) EV_NOEXCEPT
2509	{	2796	{
2510	unsigned int flags = ev_supported_backends ();	2797	unsigned int flags = ev_supported_backends ();
2511		2798
2512	#ifndef __NetBSD__	2799	#ifndef __NetBSD__
2513	/* kqueue is borked on everything but netbsd apparently */	2800	/* kqueue is borked on everything but netbsd apparently */
…		…
2521	#endif	2808	#endif
2522	#ifdef __FreeBSD__	2809	#ifdef __FreeBSD__
2523	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */	2810	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */
2524	#endif	2811	#endif
2525		2812
		2813	/* TODO: linuxaio is very experimental */
		2814	#if !EV_RECOMMEND_LINUXAIO
		2815	flags &= ~EVBACKEND_LINUXAIO;
		2816	#endif
		2817
2526	return flags;	2818	return flags;
2527	}	2819	}
2528		2820
2529	unsigned int ecb_cold	2821	ecb_cold
		2822	unsigned int
2530	ev_embeddable_backends (void) EV_THROW	2823	ev_embeddable_backends (void) EV_NOEXCEPT
2531	{	2824	{
2532	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;	2825	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;
2533		2826
2534	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */	2827	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */
2535	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */	2828	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */
…		…
2537		2830
2538	return flags;	2831	return flags;
2539	}	2832	}
2540		2833
2541	unsigned int	2834	unsigned int
2542	ev_backend (EV_P) EV_THROW	2835	ev_backend (EV_P) EV_NOEXCEPT
2543	{	2836	{
2544	return backend;	2837	return backend;
2545	}	2838	}
2546		2839
2547	#if EV_FEATURE_API	2840	#if EV_FEATURE_API
2548	unsigned int	2841	unsigned int
2549	ev_iteration (EV_P) EV_THROW	2842	ev_iteration (EV_P) EV_NOEXCEPT
2550	{	2843	{
2551	return loop_count;	2844	return loop_count;
2552	}	2845	}
2553		2846
2554	unsigned int	2847	unsigned int
2555	ev_depth (EV_P) EV_THROW	2848	ev_depth (EV_P) EV_NOEXCEPT
2556	{	2849	{
2557	return loop_depth;	2850	return loop_depth;
2558	}	2851	}
2559		2852
2560	void	2853	void
2561	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2854	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2562	{	2855	{
2563	io_blocktime = interval;	2856	io_blocktime = interval;
2564	}	2857	}
2565		2858
2566	void	2859	void
2567	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	2860	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2568	{	2861	{
2569	timeout_blocktime = interval;	2862	timeout_blocktime = interval;
2570	}	2863	}
2571		2864
2572	void	2865	void
2573	ev_set_userdata (EV_P_ void *data) EV_THROW	2866	ev_set_userdata (EV_P_ void *data) EV_NOEXCEPT
2574	{	2867	{
2575	userdata = data;	2868	userdata = data;
2576	}	2869	}
2577		2870
2578	void *	2871	void *
2579	ev_userdata (EV_P) EV_THROW	2872	ev_userdata (EV_P) EV_NOEXCEPT
2580	{	2873	{
2581	return userdata;	2874	return userdata;
2582	}	2875	}
2583		2876
2584	void	2877	void
2585	ev_set_invoke_pending_cb (EV_P_ ev_loop_callback invoke_pending_cb) EV_THROW	2878	ev_set_invoke_pending_cb (EV_P_ ev_loop_callback invoke_pending_cb) EV_NOEXCEPT
2586	{	2879	{
2587	invoke_cb = invoke_pending_cb;	2880	invoke_cb = invoke_pending_cb;
2588	}	2881	}
2589		2882
2590	void	2883	void
2591	ev_set_loop_release_cb (EV_P_ ev_loop_callback_nothrow release, ev_loop_callback_nothrow acquire) EV_THROW	2884	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_NOEXCEPT, void (*acquire)(EV_P) EV_NOEXCEPT) EV_NOEXCEPT
2592	{	2885	{
2593	release_cb = release;	2886	release_cb = release;
2594	acquire_cb = acquire;	2887	acquire_cb = acquire;
2595	}	2888	}
2596	#endif	2889	#endif
2597		2890
2598	/* initialise a loop structure, must be zero-initialised */	2891	/* initialise a loop structure, must be zero-initialised */
2599	static void noinline ecb_cold	2892	noinline ecb_cold
		2893	static void
2600	loop_init (EV_P_ unsigned int flags) EV_THROW	2894	loop_init (EV_P_ unsigned int flags) EV_NOEXCEPT
2601	{	2895	{
2602	if (!backend)	2896	if (!backend)
2603	{	2897	{
2604	origflags = flags;	2898	origflags = flags;
2605		2899
…		…
2663		2957
2664	if (!(flags & EVBACKEND_MASK))	2958	if (!(flags & EVBACKEND_MASK))
2665	flags |= ev_recommended_backends ();	2959	flags |= ev_recommended_backends ();
2666		2960
2667	#if EV_USE_IOCP	2961	#if EV_USE_IOCP
2668	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);	2962	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);
2669	#endif	2963	#endif
2670	#if EV_USE_PORT	2964	#if EV_USE_PORT
2671	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);	2965	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);
2672	#endif	2966	#endif
2673	#if EV_USE_KQUEUE	2967	#if EV_USE_KQUEUE
2674	if (!backend && (flags & EVBACKEND_KQUEUE)) backend = kqueue_init (EV_A_ flags);	2968	if (!backend && (flags & EVBACKEND_KQUEUE )) backend = kqueue_init (EV_A_ flags);
		2969	#endif
		2970	#if EV_USE_LINUXAIO
		2971	if (!backend && (flags & EVBACKEND_LINUXAIO)) backend = linuxaio_init (EV_A_ flags);
2675	#endif	2972	#endif
2676	#if EV_USE_EPOLL	2973	#if EV_USE_EPOLL
2677	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);	2974	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);
2678	#endif	2975	#endif
2679	#if EV_USE_POLL	2976	#if EV_USE_POLL
2680	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);	2977	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);
2681	#endif	2978	#endif
2682	#if EV_USE_SELECT	2979	#if EV_USE_SELECT
2683	if (!backend && (flags & EVBACKEND_SELECT)) backend = select_init (EV_A_ flags);	2980	if (!backend && (flags & EVBACKEND_SELECT )) backend = select_init (EV_A_ flags);
2684	#endif	2981	#endif
2685		2982
2686	ev_prepare_init (&pending_w, pendingcb);	2983	ev_prepare_init (&pending_w, pendingcb);
2687		2984
2688	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	2985	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
…		…
2691	#endif	2988	#endif
2692	}	2989	}
2693	}	2990	}
2694		2991
2695	/* free up a loop structure */	2992	/* free up a loop structure */
2696	void ecb_cold	2993	ecb_cold
		2994	void
2697	ev_loop_destroy (EV_P)	2995	ev_loop_destroy (EV_P)
2698	{	2996	{
2699	int i;	2997	int i;
2700		2998
2701	#if EV_MULTIPLICITY	2999	#if EV_MULTIPLICITY
…		…
2742		3040
2743	if (backend_fd >= 0)	3041	if (backend_fd >= 0)
2744	close (backend_fd);	3042	close (backend_fd);
2745		3043
2746	#if EV_USE_IOCP	3044	#if EV_USE_IOCP
2747	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);	3045	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);
2748	#endif	3046	#endif
2749	#if EV_USE_PORT	3047	#if EV_USE_PORT
2750	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);	3048	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);
2751	#endif	3049	#endif
2752	#if EV_USE_KQUEUE	3050	#if EV_USE_KQUEUE
2753	if (backend == EVBACKEND_KQUEUE) kqueue_destroy (EV_A);	3051	if (backend == EVBACKEND_KQUEUE ) kqueue_destroy (EV_A);
		3052	#endif
		3053	#if EV_USE_LINUXAIO
		3054	if (backend == EVBACKEND_LINUXAIO) linuxaio_destroy (EV_A);
2754	#endif	3055	#endif
2755	#if EV_USE_EPOLL	3056	#if EV_USE_EPOLL
2756	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);	3057	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);
2757	#endif	3058	#endif
2758	#if EV_USE_POLL	3059	#if EV_USE_POLL
2759	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);	3060	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);
2760	#endif	3061	#endif
2761	#if EV_USE_SELECT	3062	#if EV_USE_SELECT
2762	if (backend == EVBACKEND_SELECT) select_destroy (EV_A);	3063	if (backend == EVBACKEND_SELECT ) select_destroy (EV_A);
2763	#endif	3064	#endif
2764		3065
2765	for (i = NUMPRI; i--; )	3066	for (i = NUMPRI; i--; )
2766	{	3067	{
2767	array_free (pending, [i]);	3068	array_free (pending, [i]);
…		…
2809		3110
2810	inline_size void	3111	inline_size void
2811	loop_fork (EV_P)	3112	loop_fork (EV_P)
2812	{	3113	{
2813	#if EV_USE_PORT	3114	#if EV_USE_PORT
2814	if (backend == EVBACKEND_PORT ) port_fork (EV_A);	3115	if (backend == EVBACKEND_PORT ) port_fork (EV_A);
2815	#endif	3116	#endif
2816	#if EV_USE_KQUEUE	3117	#if EV_USE_KQUEUE
2817	if (backend == EVBACKEND_KQUEUE) kqueue_fork (EV_A);	3118	if (backend == EVBACKEND_KQUEUE ) kqueue_fork (EV_A);
		3119	#endif
		3120	#if EV_USE_LINUXAIO
		3121	if (backend == EVBACKEND_LINUXAIO) linuxaio_fork (EV_A);
2818	#endif	3122	#endif
2819	#if EV_USE_EPOLL	3123	#if EV_USE_EPOLL
2820	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);	3124	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);
2821	#endif	3125	#endif
2822	#if EV_USE_INOTIFY	3126	#if EV_USE_INOTIFY
2823	infy_fork (EV_A);	3127	infy_fork (EV_A);
2824	#endif	3128	#endif
2825		3129
2826	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	3130	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2827	if (ev_is_active (&pipe_w))	3131	if (ev_is_active (&pipe_w) && postfork != 2)
2828	{	3132	{
2829	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */	3133	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */
2830		3134
2831	ev_ref (EV_A);	3135	ev_ref (EV_A);
2832	ev_io_stop (EV_A_ &pipe_w);	3136	ev_io_stop (EV_A_ &pipe_w);
…		…
2843	postfork = 0;	3147	postfork = 0;
2844	}	3148	}
2845		3149
2846	#if EV_MULTIPLICITY	3150	#if EV_MULTIPLICITY
2847		3151
		3152	ecb_cold
2848	struct ev_loop * ecb_cold	3153	struct ev_loop *
2849	ev_loop_new (unsigned int flags) EV_THROW	3154	ev_loop_new (unsigned int flags) EV_NOEXCEPT
2850	{	3155	{
2851	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));	3156	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));
2852		3157
2853	memset (EV_A, 0, sizeof (struct ev_loop));	3158	memset (EV_A, 0, sizeof (struct ev_loop));
2854	loop_init (EV_A_ flags);	3159	loop_init (EV_A_ flags);
…		…
2861	}	3166	}
2862		3167
2863	#endif /* multiplicity */	3168	#endif /* multiplicity */
2864		3169
2865	#if EV_VERIFY	3170	#if EV_VERIFY
2866	static void noinline ecb_cold	3171	noinline ecb_cold
		3172	static void
2867	verify_watcher (EV_P_ W w)	3173	verify_watcher (EV_P_ W w)
2868	{	3174	{
2869	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));	3175	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));
2870		3176
2871	if (w->pending)	3177	if (w->pending)
2872	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));	3178	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));
2873	}	3179	}
2874		3180
2875	static void noinline ecb_cold	3181	noinline ecb_cold
		3182	static void
2876	verify_heap (EV_P_ ANHE *heap, int N)	3183	verify_heap (EV_P_ ANHE *heap, int N)
2877	{	3184	{
2878	int i;	3185	int i;
2879		3186
2880	for (i = HEAP0; i < N + HEAP0; ++i)	3187	for (i = HEAP0; i < N + HEAP0; ++i)
…		…
2885		3192
2886	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));	3193	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));
2887	}	3194	}
2888	}	3195	}
2889		3196
2890	static void noinline ecb_cold	3197	noinline ecb_cold
		3198	static void
2891	array_verify (EV_P_ W *ws, int cnt)	3199	array_verify (EV_P_ W *ws, int cnt)
2892	{	3200	{
2893	while (cnt--)	3201	while (cnt--)
2894	{	3202	{
2895	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));	3203	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));
…		…
2898	}	3206	}
2899	#endif	3207	#endif
2900		3208
2901	#if EV_FEATURE_API	3209	#if EV_FEATURE_API
2902	void ecb_cold	3210	void ecb_cold
2903	ev_verify (EV_P) EV_THROW	3211	ev_verify (EV_P) EV_NOEXCEPT
2904	{	3212	{
2905	#if EV_VERIFY	3213	#if EV_VERIFY
2906	int i;	3214	int i;
2907	WL w, w2;	3215	WL w, w2;
2908		3216
…		…
2984	#endif	3292	#endif
2985	}	3293	}
2986	#endif	3294	#endif
2987		3295
2988	#if EV_MULTIPLICITY	3296	#if EV_MULTIPLICITY
		3297	ecb_cold
2989	struct ev_loop * ecb_cold	3298	struct ev_loop *
2990	#else	3299	#else
2991	int	3300	int
2992	#endif	3301	#endif
2993	ev_default_loop (unsigned int flags) EV_THROW	3302	ev_default_loop (unsigned int flags) EV_NOEXCEPT
2994	{	3303	{
2995	if (!ev_default_loop_ptr)	3304	if (!ev_default_loop_ptr)
2996	{	3305	{
2997	#if EV_MULTIPLICITY	3306	#if EV_MULTIPLICITY
2998	EV_P = ev_default_loop_ptr = &default_loop_struct;	3307	EV_P = ev_default_loop_ptr = &default_loop_struct;
…		…
3017		3326
3018	return ev_default_loop_ptr;	3327	return ev_default_loop_ptr;
3019	}	3328	}
3020		3329
3021	void	3330	void
3022	ev_loop_fork (EV_P) EV_THROW	3331	ev_loop_fork (EV_P) EV_NOEXCEPT
3023	{	3332	{
3024	postfork = 1;	3333	postfork = 1;
3025	}	3334	}
3026		3335
3027	/*****************************************************************************/	3336	/*****************************************************************************/
…		…
3031	{	3340	{
3032	EV_CB_INVOKE ((W)w, revents);	3341	EV_CB_INVOKE ((W)w, revents);
3033	}	3342	}
3034		3343
3035	unsigned int	3344	unsigned int
3036	ev_pending_count (EV_P) EV_THROW	3345	ev_pending_count (EV_P) EV_NOEXCEPT
3037	{	3346	{
3038	int pri;	3347	int pri;
3039	unsigned int count = 0;	3348	unsigned int count = 0;
3040		3349
3041	for (pri = NUMPRI; pri--; )	3350	for (pri = NUMPRI; pri--; )
3042	count += pendingcnt [pri];	3351	count += pendingcnt [pri];
3043		3352
3044	return count;	3353	return count;
3045	}	3354	}
3046		3355
3047	void noinline	3356	noinline
		3357	void
3048	ev_invoke_pending (EV_P)	3358	ev_invoke_pending (EV_P)
3049	{	3359	{
3050	pendingpri = NUMPRI;	3360	pendingpri = NUMPRI;
3051		3361
3052	while (pendingpri) /* pendingpri possibly gets modified in the inner loop */	3362	do
3053	{	3363	{
3054	--pendingpri;	3364	--pendingpri;
3055		3365
		3366	/* pendingpri possibly gets modified in the inner loop */
3056	while (pendingcnt [pendingpri])	3367	while (pendingcnt [pendingpri])
3057	{	3368	{
3058	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];	3369	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];
3059		3370
3060	p->w->pending = 0;	3371	p->w->pending = 0;
3061	EV_CB_INVOKE (p->w, p->events);	3372	EV_CB_INVOKE (p->w, p->events);
3062	EV_FREQUENT_CHECK;	3373	EV_FREQUENT_CHECK;
3063	}	3374	}
3064	}	3375	}
		3376	while (pendingpri);
3065	}	3377	}
3066		3378
3067	#if EV_IDLE_ENABLE	3379	#if EV_IDLE_ENABLE
3068	/* make idle watchers pending. this handles the "call-idle */	3380	/* make idle watchers pending. this handles the "call-idle */
3069	/* only when higher priorities are idle" logic */	3381	/* only when higher priorities are idle" logic */
…		…
3127	}	3439	}
3128	}	3440	}
3129		3441
3130	#if EV_PERIODIC_ENABLE	3442	#if EV_PERIODIC_ENABLE
3131		3443
3132	static void noinline	3444	noinline
		3445	static void
3133	periodic_recalc (EV_P_ ev_periodic *w)	3446	periodic_recalc (EV_P_ ev_periodic *w)
3134	{	3447	{
3135	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;	3448	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);	3449	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);
3137		3450
…		…
3195	}	3508	}
3196	}	3509	}
3197		3510
3198	/* simply recalculate all periodics */	3511	/* simply recalculate all periodics */
3199	/* TODO: maybe ensure that at least one event happens when jumping forward? */	3512	/* TODO: maybe ensure that at least one event happens when jumping forward? */
3200	static void noinline ecb_cold	3513	noinline ecb_cold
		3514	static void
3201	periodics_reschedule (EV_P)	3515	periodics_reschedule (EV_P)
3202	{	3516	{
3203	int i;	3517	int i;
3204		3518
3205	/* adjust periodics after time jump */	3519	/* adjust periodics after time jump */
…		…
3218	reheap (periodics, periodiccnt);	3532	reheap (periodics, periodiccnt);
3219	}	3533	}
3220	#endif	3534	#endif
3221		3535
3222	/* adjust all timers by a given offset */	3536	/* adjust all timers by a given offset */
3223	static void noinline ecb_cold	3537	noinline ecb_cold
		3538	static void
3224	timers_reschedule (EV_P_ ev_tstamp adjust)	3539	timers_reschedule (EV_P_ ev_tstamp adjust)
3225	{	3540	{
3226	int i;	3541	int i;
3227		3542
3228	for (i = 0; i < timercnt; ++i)	3543	for (i = 0; i < timercnt; ++i)
…		…
3475		3790
3476	return activecnt;	3791	return activecnt;
3477	}	3792	}
3478		3793
3479	void	3794	void
3480	ev_break (EV_P_ int how) EV_THROW	3795	ev_break (EV_P_ int how) EV_NOEXCEPT
3481	{	3796	{
3482	loop_done = how;	3797	loop_done = how;
3483	}	3798	}
3484		3799
3485	void	3800	void
3486	ev_ref (EV_P) EV_THROW	3801	ev_ref (EV_P) EV_NOEXCEPT
3487	{	3802	{
3488	++activecnt;	3803	++activecnt;
3489	}	3804	}
3490		3805
3491	void	3806	void
3492	ev_unref (EV_P) EV_THROW	3807	ev_unref (EV_P) EV_NOEXCEPT
3493	{	3808	{
3494	--activecnt;	3809	--activecnt;
3495	}	3810	}
3496		3811
3497	void	3812	void
3498	ev_now_update (EV_P) EV_THROW	3813	ev_now_update (EV_P) EV_NOEXCEPT
3499	{	3814	{
3500	time_update (EV_A_ 1e100);	3815	time_update (EV_A_ 1e100);
3501	}	3816	}
3502		3817
3503	void	3818	void
3504	ev_suspend (EV_P) EV_THROW	3819	ev_suspend (EV_P) EV_NOEXCEPT
3505	{	3820	{
3506	ev_now_update (EV_A);	3821	ev_now_update (EV_A);
3507	}	3822	}
3508		3823
3509	void	3824	void
3510	ev_resume (EV_P) EV_THROW	3825	ev_resume (EV_P) EV_NOEXCEPT
3511	{	3826	{
3512	ev_tstamp mn_prev = mn_now;	3827	ev_tstamp mn_prev = mn_now;
3513		3828
3514	ev_now_update (EV_A);	3829	ev_now_update (EV_A);
3515	timers_reschedule (EV_A_ mn_now - mn_prev);	3830	timers_reschedule (EV_A_ mn_now - mn_prev);
…		…
3554	w->pending = 0;	3869	w->pending = 0;
3555	}	3870	}
3556	}	3871	}
3557		3872
3558	int	3873	int
3559	ev_clear_pending (EV_P_ void *w) EV_THROW	3874	ev_clear_pending (EV_P_ void *w) EV_NOEXCEPT
3560	{	3875	{
3561	W w_ = (W)w;	3876	W w_ = (W)w;
3562	int pending = w_->pending;	3877	int pending = w_->pending;
3563		3878
3564	if (expect_true (pending))	3879	if (expect_true (pending))
…		…
3596	w->active = 0;	3911	w->active = 0;
3597	}	3912	}
3598		3913
3599	/*****************************************************************************/	3914	/*****************************************************************************/
3600		3915
3601	void noinline	3916	noinline
		3917	void
3602	ev_io_start (EV_P_ ev_io *w) EV_THROW	3918	ev_io_start (EV_P_ ev_io *w) EV_NOEXCEPT
3603	{	3919	{
3604	int fd = w->fd;	3920	int fd = w->fd;
3605		3921
3606	if (expect_false (ev_is_active (w)))	3922	if (expect_false (ev_is_active (w)))
3607	return;	3923	return;
…		…
3610	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));	3926	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));
3611		3927
3612	EV_FREQUENT_CHECK;	3928	EV_FREQUENT_CHECK;
3613		3929
3614	ev_start (EV_A_ (W)w, 1);	3930	ev_start (EV_A_ (W)w, 1);
3615	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_init_zero);	3931	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_needsize_zerofill);
3616	wlist_add (&anfds[fd].head, (WL)w);	3932	wlist_add (&anfds[fd].head, (WL)w);
3617		3933
3618	/* common bug, apparently */	3934	/* common bug, apparently */
3619	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));	3935	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));
3620		3936
…		…
3622	w->events &= ~EV__IOFDSET;	3938	w->events &= ~EV__IOFDSET;
3623		3939
3624	EV_FREQUENT_CHECK;	3940	EV_FREQUENT_CHECK;
3625	}	3941	}
3626		3942
3627	void noinline	3943	noinline
		3944	void
3628	ev_io_stop (EV_P_ ev_io *w) EV_THROW	3945	ev_io_stop (EV_P_ ev_io *w) EV_NOEXCEPT
3629	{	3946	{
3630	clear_pending (EV_A_ (W)w);	3947	clear_pending (EV_A_ (W)w);
3631	if (expect_false (!ev_is_active (w)))	3948	if (expect_false (!ev_is_active (w)))
3632	return;	3949	return;
3633		3950
…		…
3641	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);	3958	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);
3642		3959
3643	EV_FREQUENT_CHECK;	3960	EV_FREQUENT_CHECK;
3644	}	3961	}
3645		3962
3646	void noinline	3963	noinline
		3964	void
3647	ev_timer_start (EV_P_ ev_timer *w) EV_THROW	3965	ev_timer_start (EV_P_ ev_timer *w) EV_NOEXCEPT
3648	{	3966	{
3649	if (expect_false (ev_is_active (w)))	3967	if (expect_false (ev_is_active (w)))
3650	return;	3968	return;
3651		3969
3652	ev_at (w) += mn_now;	3970	ev_at (w) += mn_now;
…		…
3655		3973
3656	EV_FREQUENT_CHECK;	3974	EV_FREQUENT_CHECK;
3657		3975
3658	++timercnt;	3976	++timercnt;
3659	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);	3977	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);
3660	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, EMPTY2);	3978	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, array_needsize_noinit);
3661	ANHE_w (timers [ev_active (w)]) = (WT)w;	3979	ANHE_w (timers [ev_active (w)]) = (WT)w;
3662	ANHE_at_cache (timers [ev_active (w)]);	3980	ANHE_at_cache (timers [ev_active (w)]);
3663	upheap (timers, ev_active (w));	3981	upheap (timers, ev_active (w));
3664		3982
3665	EV_FREQUENT_CHECK;	3983	EV_FREQUENT_CHECK;
3666		3984
3667	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/	3985	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/
3668	}	3986	}
3669		3987
3670	void noinline	3988	noinline
		3989	void
3671	ev_timer_stop (EV_P_ ev_timer *w) EV_THROW	3990	ev_timer_stop (EV_P_ ev_timer *w) EV_NOEXCEPT
3672	{	3991	{
3673	clear_pending (EV_A_ (W)w);	3992	clear_pending (EV_A_ (W)w);
3674	if (expect_false (!ev_is_active (w)))	3993	if (expect_false (!ev_is_active (w)))
3675	return;	3994	return;
3676		3995
…		…
3695	ev_stop (EV_A_ (W)w);	4014	ev_stop (EV_A_ (W)w);
3696		4015
3697	EV_FREQUENT_CHECK;	4016	EV_FREQUENT_CHECK;
3698	}	4017	}
3699		4018
3700	void noinline	4019	noinline
		4020	void
3701	ev_timer_again (EV_P_ ev_timer *w) EV_THROW	4021	ev_timer_again (EV_P_ ev_timer *w) EV_NOEXCEPT
3702	{	4022	{
3703	EV_FREQUENT_CHECK;	4023	EV_FREQUENT_CHECK;
3704		4024
3705	clear_pending (EV_A_ (W)w);	4025	clear_pending (EV_A_ (W)w);
3706		4026
…		…
3723		4043
3724	EV_FREQUENT_CHECK;	4044	EV_FREQUENT_CHECK;
3725	}	4045	}
3726		4046
3727	ev_tstamp	4047	ev_tstamp
3728	ev_timer_remaining (EV_P_ ev_timer *w) EV_THROW	4048	ev_timer_remaining (EV_P_ ev_timer *w) EV_NOEXCEPT
3729	{	4049	{
3730	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);	4050	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);
3731	}	4051	}
3732		4052
3733	#if EV_PERIODIC_ENABLE	4053	#if EV_PERIODIC_ENABLE
3734	void noinline	4054	noinline
		4055	void
3735	ev_periodic_start (EV_P_ ev_periodic *w) EV_THROW	4056	ev_periodic_start (EV_P_ ev_periodic *w) EV_NOEXCEPT
3736	{	4057	{
3737	if (expect_false (ev_is_active (w)))	4058	if (expect_false (ev_is_active (w)))
3738	return;	4059	return;
3739		4060
3740	if (w->reschedule_cb)	4061	if (w->reschedule_cb)
…		…
3749		4070
3750	EV_FREQUENT_CHECK;	4071	EV_FREQUENT_CHECK;
3751		4072
3752	++periodiccnt;	4073	++periodiccnt;
3753	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);	4074	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);
3754	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, EMPTY2);	4075	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, array_needsize_noinit);
3755	ANHE_w (periodics [ev_active (w)]) = (WT)w;	4076	ANHE_w (periodics [ev_active (w)]) = (WT)w;
3756	ANHE_at_cache (periodics [ev_active (w)]);	4077	ANHE_at_cache (periodics [ev_active (w)]);
3757	upheap (periodics, ev_active (w));	4078	upheap (periodics, ev_active (w));
3758		4079
3759	EV_FREQUENT_CHECK;	4080	EV_FREQUENT_CHECK;
3760		4081
3761	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/	4082	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/
3762	}	4083	}
3763		4084
3764	void noinline	4085	noinline
		4086	void
3765	ev_periodic_stop (EV_P_ ev_periodic *w) EV_THROW	4087	ev_periodic_stop (EV_P_ ev_periodic *w) EV_NOEXCEPT
3766	{	4088	{
3767	clear_pending (EV_A_ (W)w);	4089	clear_pending (EV_A_ (W)w);
3768	if (expect_false (!ev_is_active (w)))	4090	if (expect_false (!ev_is_active (w)))
3769	return;	4091	return;
3770		4092
…		…
3787	ev_stop (EV_A_ (W)w);	4109	ev_stop (EV_A_ (W)w);
3788		4110
3789	EV_FREQUENT_CHECK;	4111	EV_FREQUENT_CHECK;
3790	}	4112	}
3791		4113
3792	void noinline	4114	noinline
		4115	void
3793	ev_periodic_again (EV_P_ ev_periodic *w) EV_THROW	4116	ev_periodic_again (EV_P_ ev_periodic *w) EV_NOEXCEPT
3794	{	4117	{
3795	/* TODO: use adjustheap and recalculation */	4118	/* TODO: use adjustheap and recalculation */
3796	ev_periodic_stop (EV_A_ w);	4119	ev_periodic_stop (EV_A_ w);
3797	ev_periodic_start (EV_A_ w);	4120	ev_periodic_start (EV_A_ w);
3798	}	4121	}
…		…
3802	# define SA_RESTART 0	4125	# define SA_RESTART 0
3803	#endif	4126	#endif
3804		4127
3805	#if EV_SIGNAL_ENABLE	4128	#if EV_SIGNAL_ENABLE
3806		4129
3807	void noinline	4130	noinline
		4131	void
3808	ev_signal_start (EV_P_ ev_signal *w) EV_THROW	4132	ev_signal_start (EV_P_ ev_signal *w) EV_NOEXCEPT
3809	{	4133	{
3810	if (expect_false (ev_is_active (w)))	4134	if (expect_false (ev_is_active (w)))
3811	return;	4135	return;
3812		4136
3813	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));	4137	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));
…		…
3884	}	4208	}
3885		4209
3886	EV_FREQUENT_CHECK;	4210	EV_FREQUENT_CHECK;
3887	}	4211	}
3888		4212
3889	void noinline	4213	noinline
		4214	void
3890	ev_signal_stop (EV_P_ ev_signal *w) EV_THROW	4215	ev_signal_stop (EV_P_ ev_signal *w) EV_NOEXCEPT
3891	{	4216	{
3892	clear_pending (EV_A_ (W)w);	4217	clear_pending (EV_A_ (W)w);
3893	if (expect_false (!ev_is_active (w)))	4218	if (expect_false (!ev_is_active (w)))
3894	return;	4219	return;
3895		4220
…		…
3926	#endif	4251	#endif
3927		4252
3928	#if EV_CHILD_ENABLE	4253	#if EV_CHILD_ENABLE
3929		4254
3930	void	4255	void
3931	ev_child_start (EV_P_ ev_child *w) EV_THROW	4256	ev_child_start (EV_P_ ev_child *w) EV_NOEXCEPT
3932	{	4257	{
3933	#if EV_MULTIPLICITY	4258	#if EV_MULTIPLICITY
3934	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));	4259	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));
3935	#endif	4260	#endif
3936	if (expect_false (ev_is_active (w)))	4261	if (expect_false (ev_is_active (w)))
…		…
3943		4268
3944	EV_FREQUENT_CHECK;	4269	EV_FREQUENT_CHECK;
3945	}	4270	}
3946		4271
3947	void	4272	void
3948	ev_child_stop (EV_P_ ev_child *w) EV_THROW	4273	ev_child_stop (EV_P_ ev_child *w) EV_NOEXCEPT
3949	{	4274	{
3950	clear_pending (EV_A_ (W)w);	4275	clear_pending (EV_A_ (W)w);
3951	if (expect_false (!ev_is_active (w)))	4276	if (expect_false (!ev_is_active (w)))
3952	return;	4277	return;
3953		4278
…		…
3970		4295
3971	#define DEF_STAT_INTERVAL 5.0074891	4296	#define DEF_STAT_INTERVAL 5.0074891
3972	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */	4297	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */
3973	#define MIN_STAT_INTERVAL 0.1074891	4298	#define MIN_STAT_INTERVAL 0.1074891
3974		4299
3975	static void noinline stat_timer_cb (EV_P_ ev_timer *w_, int revents);	4300	noinline static void stat_timer_cb (EV_P_ ev_timer *w_, int revents);
3976		4301
3977	#if EV_USE_INOTIFY	4302	#if EV_USE_INOTIFY
3978		4303
3979	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */	4304	/* 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)	4305	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)
3981		4306
3982	static void noinline	4307	noinline
		4308	static void
3983	infy_add (EV_P_ ev_stat *w)	4309	infy_add (EV_P_ ev_stat *w)
3984	{	4310	{
3985	w->wd = inotify_add_watch (fs_fd, w->path,	4311	w->wd = inotify_add_watch (fs_fd, w->path,
3986	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY	4312	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY
3987	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO	4313	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO
…		…
4051	if (ev_is_active (&w->timer)) ev_ref (EV_A);	4377	if (ev_is_active (&w->timer)) ev_ref (EV_A);
4052	ev_timer_again (EV_A_ &w->timer);	4378	ev_timer_again (EV_A_ &w->timer);
4053	if (ev_is_active (&w->timer)) ev_unref (EV_A);	4379	if (ev_is_active (&w->timer)) ev_unref (EV_A);
4054	}	4380	}
4055		4381
4056	static void noinline	4382	noinline
		4383	static void
4057	infy_del (EV_P_ ev_stat *w)	4384	infy_del (EV_P_ ev_stat *w)
4058	{	4385	{
4059	int slot;	4386	int slot;
4060	int wd = w->wd;	4387	int wd = w->wd;
4061		4388
…		…
4068		4395
4069	/* remove this watcher, if others are watching it, they will rearm */	4396	/* remove this watcher, if others are watching it, they will rearm */
4070	inotify_rm_watch (fs_fd, wd);	4397	inotify_rm_watch (fs_fd, wd);
4071	}	4398	}
4072		4399
4073	static void noinline	4400	noinline
		4401	static void
4074	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)	4402	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)
4075	{	4403	{
4076	if (slot < 0)	4404	if (slot < 0)
4077	/* overflow, need to check for all hash slots */	4405	/* overflow, need to check for all hash slots */
4078	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)	4406	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)
…		…
4114	infy_wd (EV_A_ ev->wd, ev->wd, ev);	4442	infy_wd (EV_A_ ev->wd, ev->wd, ev);
4115	ofs += sizeof (struct inotify_event) + ev->len;	4443	ofs += sizeof (struct inotify_event) + ev->len;
4116	}	4444	}
4117	}	4445	}
4118		4446
4119	inline_size void ecb_cold	4447	inline_size ecb_cold
		4448	void
4120	ev_check_2625 (EV_P)	4449	ev_check_2625 (EV_P)
4121	{	4450	{
4122	/* kernels < 2.6.25 are borked	4451	/* kernels < 2.6.25 are borked
4123	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html	4452	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html
4124	*/	4453	*/
…		…
4214	#else	4543	#else
4215	# define EV_LSTAT(p,b) lstat (p, b)	4544	# define EV_LSTAT(p,b) lstat (p, b)
4216	#endif	4545	#endif
4217		4546
4218	void	4547	void
4219	ev_stat_stat (EV_P_ ev_stat *w) EV_THROW	4548	ev_stat_stat (EV_P_ ev_stat *w) EV_NOEXCEPT
4220	{	4549	{
4221	if (lstat (w->path, &w->attr) < 0)	4550	if (lstat (w->path, &w->attr) < 0)
4222	w->attr.st_nlink = 0;	4551	w->attr.st_nlink = 0;
4223	else if (!w->attr.st_nlink)	4552	else if (!w->attr.st_nlink)
4224	w->attr.st_nlink = 1;	4553	w->attr.st_nlink = 1;
4225	}	4554	}
4226		4555
4227	static void noinline	4556	noinline
		4557	static void
4228	stat_timer_cb (EV_P_ ev_timer *w_, int revents)	4558	stat_timer_cb (EV_P_ ev_timer *w_, int revents)
4229	{	4559	{
4230	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));	4560	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));
4231		4561
4232	ev_statdata prev = w->attr;	4562	ev_statdata prev = w->attr;
…		…
4263	ev_feed_event (EV_A_ w, EV_STAT);	4593	ev_feed_event (EV_A_ w, EV_STAT);
4264	}	4594	}
4265	}	4595	}
4266		4596
4267	void	4597	void
4268	ev_stat_start (EV_P_ ev_stat *w) EV_THROW	4598	ev_stat_start (EV_P_ ev_stat *w) EV_NOEXCEPT
4269	{	4599	{
4270	if (expect_false (ev_is_active (w)))	4600	if (expect_false (ev_is_active (w)))
4271	return;	4601	return;
4272		4602
4273	ev_stat_stat (EV_A_ w);	4603	ev_stat_stat (EV_A_ w);
…		…
4294		4624
4295	EV_FREQUENT_CHECK;	4625	EV_FREQUENT_CHECK;
4296	}	4626	}
4297		4627
4298	void	4628	void
4299	ev_stat_stop (EV_P_ ev_stat *w) EV_THROW	4629	ev_stat_stop (EV_P_ ev_stat *w) EV_NOEXCEPT
4300	{	4630	{
4301	clear_pending (EV_A_ (W)w);	4631	clear_pending (EV_A_ (W)w);
4302	if (expect_false (!ev_is_active (w)))	4632	if (expect_false (!ev_is_active (w)))
4303	return;	4633	return;
4304		4634
…		…
4320	}	4650	}
4321	#endif	4651	#endif
4322		4652
4323	#if EV_IDLE_ENABLE	4653	#if EV_IDLE_ENABLE
4324	void	4654	void
4325	ev_idle_start (EV_P_ ev_idle *w) EV_THROW	4655	ev_idle_start (EV_P_ ev_idle *w) EV_NOEXCEPT
4326	{	4656	{
4327	if (expect_false (ev_is_active (w)))	4657	if (expect_false (ev_is_active (w)))
4328	return;	4658	return;
4329		4659
4330	pri_adjust (EV_A_ (W)w);	4660	pri_adjust (EV_A_ (W)w);
…		…
4335	int active = ++idlecnt [ABSPRI (w)];	4665	int active = ++idlecnt [ABSPRI (w)];
4336		4666
4337	++idleall;	4667	++idleall;
4338	ev_start (EV_A_ (W)w, active);	4668	ev_start (EV_A_ (W)w, active);
4339		4669
4340	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, EMPTY2);	4670	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, array_needsize_noinit);
4341	idles [ABSPRI (w)][active - 1] = w;	4671	idles [ABSPRI (w)][active - 1] = w;
4342	}	4672	}
4343		4673
4344	EV_FREQUENT_CHECK;	4674	EV_FREQUENT_CHECK;
4345	}	4675	}
4346		4676
4347	void	4677	void
4348	ev_idle_stop (EV_P_ ev_idle *w) EV_THROW	4678	ev_idle_stop (EV_P_ ev_idle *w) EV_NOEXCEPT
4349	{	4679	{
4350	clear_pending (EV_A_ (W)w);	4680	clear_pending (EV_A_ (W)w);
4351	if (expect_false (!ev_is_active (w)))	4681	if (expect_false (!ev_is_active (w)))
4352	return;	4682	return;
4353		4683
…		…
4367	}	4697	}
4368	#endif	4698	#endif
4369		4699
4370	#if EV_PREPARE_ENABLE	4700	#if EV_PREPARE_ENABLE
4371	void	4701	void
4372	ev_prepare_start (EV_P_ ev_prepare *w) EV_THROW	4702	ev_prepare_start (EV_P_ ev_prepare *w) EV_NOEXCEPT
4373	{	4703	{
4374	if (expect_false (ev_is_active (w)))	4704	if (expect_false (ev_is_active (w)))
4375	return;	4705	return;
4376		4706
4377	EV_FREQUENT_CHECK;	4707	EV_FREQUENT_CHECK;
4378		4708
4379	ev_start (EV_A_ (W)w, ++preparecnt);	4709	ev_start (EV_A_ (W)w, ++preparecnt);
4380	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, EMPTY2);	4710	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, array_needsize_noinit);
4381	prepares [preparecnt - 1] = w;	4711	prepares [preparecnt - 1] = w;
4382		4712
4383	EV_FREQUENT_CHECK;	4713	EV_FREQUENT_CHECK;
4384	}	4714	}
4385		4715
4386	void	4716	void
4387	ev_prepare_stop (EV_P_ ev_prepare *w) EV_THROW	4717	ev_prepare_stop (EV_P_ ev_prepare *w) EV_NOEXCEPT
4388	{	4718	{
4389	clear_pending (EV_A_ (W)w);	4719	clear_pending (EV_A_ (W)w);
4390	if (expect_false (!ev_is_active (w)))	4720	if (expect_false (!ev_is_active (w)))
4391	return;	4721	return;
4392		4722
…		…
4405	}	4735	}
4406	#endif	4736	#endif
4407		4737
4408	#if EV_CHECK_ENABLE	4738	#if EV_CHECK_ENABLE
4409	void	4739	void
4410	ev_check_start (EV_P_ ev_check *w) EV_THROW	4740	ev_check_start (EV_P_ ev_check *w) EV_NOEXCEPT
4411	{	4741	{
4412	if (expect_false (ev_is_active (w)))	4742	if (expect_false (ev_is_active (w)))
4413	return;	4743	return;
4414		4744
4415	EV_FREQUENT_CHECK;	4745	EV_FREQUENT_CHECK;
4416		4746
4417	ev_start (EV_A_ (W)w, ++checkcnt);	4747	ev_start (EV_A_ (W)w, ++checkcnt);
4418	array_needsize (ev_check *, checks, checkmax, checkcnt, EMPTY2);	4748	array_needsize (ev_check *, checks, checkmax, checkcnt, array_needsize_noinit);
4419	checks [checkcnt - 1] = w;	4749	checks [checkcnt - 1] = w;
4420		4750
4421	EV_FREQUENT_CHECK;	4751	EV_FREQUENT_CHECK;
4422	}	4752	}
4423		4753
4424	void	4754	void
4425	ev_check_stop (EV_P_ ev_check *w) EV_THROW	4755	ev_check_stop (EV_P_ ev_check *w) EV_NOEXCEPT
4426	{	4756	{
4427	clear_pending (EV_A_ (W)w);	4757	clear_pending (EV_A_ (W)w);
4428	if (expect_false (!ev_is_active (w)))	4758	if (expect_false (!ev_is_active (w)))
4429	return;	4759	return;
4430		4760
…		…
4442	EV_FREQUENT_CHECK;	4772	EV_FREQUENT_CHECK;
4443	}	4773	}
4444	#endif	4774	#endif
4445		4775
4446	#if EV_EMBED_ENABLE	4776	#if EV_EMBED_ENABLE
4447	void noinline	4777	noinline
		4778	void
4448	ev_embed_sweep (EV_P_ ev_embed *w) EV_THROW	4779	ev_embed_sweep (EV_P_ ev_embed *w) EV_NOEXCEPT
4449	{	4780	{
4450	ev_run (w->other, EVRUN_NOWAIT);	4781	ev_run (w->other, EVRUN_NOWAIT);
4451	}	4782	}
4452		4783
4453	static void	4784	static void
…		…
4501	ev_idle_stop (EV_A_ idle);	4832	ev_idle_stop (EV_A_ idle);
4502	}	4833	}
4503	#endif	4834	#endif
4504		4835
4505	void	4836	void
4506	ev_embed_start (EV_P_ ev_embed *w) EV_THROW	4837	ev_embed_start (EV_P_ ev_embed *w) EV_NOEXCEPT
4507	{	4838	{
4508	if (expect_false (ev_is_active (w)))	4839	if (expect_false (ev_is_active (w)))
4509	return;	4840	return;
4510		4841
4511	{	4842	{
…		…
4532		4863
4533	EV_FREQUENT_CHECK;	4864	EV_FREQUENT_CHECK;
4534	}	4865	}
4535		4866
4536	void	4867	void
4537	ev_embed_stop (EV_P_ ev_embed *w) EV_THROW	4868	ev_embed_stop (EV_P_ ev_embed *w) EV_NOEXCEPT
4538	{	4869	{
4539	clear_pending (EV_A_ (W)w);	4870	clear_pending (EV_A_ (W)w);
4540	if (expect_false (!ev_is_active (w)))	4871	if (expect_false (!ev_is_active (w)))
4541	return;	4872	return;
4542		4873
…		…
4552	}	4883	}
4553	#endif	4884	#endif
4554		4885
4555	#if EV_FORK_ENABLE	4886	#if EV_FORK_ENABLE
4556	void	4887	void
4557	ev_fork_start (EV_P_ ev_fork *w) EV_THROW	4888	ev_fork_start (EV_P_ ev_fork *w) EV_NOEXCEPT
4558	{	4889	{
4559	if (expect_false (ev_is_active (w)))	4890	if (expect_false (ev_is_active (w)))
4560	return;	4891	return;
4561		4892
4562	EV_FREQUENT_CHECK;	4893	EV_FREQUENT_CHECK;
4563		4894
4564	ev_start (EV_A_ (W)w, ++forkcnt);	4895	ev_start (EV_A_ (W)w, ++forkcnt);
4565	array_needsize (ev_fork *, forks, forkmax, forkcnt, EMPTY2);	4896	array_needsize (ev_fork *, forks, forkmax, forkcnt, array_needsize_noinit);
4566	forks [forkcnt - 1] = w;	4897	forks [forkcnt - 1] = w;
4567		4898
4568	EV_FREQUENT_CHECK;	4899	EV_FREQUENT_CHECK;
4569	}	4900	}
4570		4901
4571	void	4902	void
4572	ev_fork_stop (EV_P_ ev_fork *w) EV_THROW	4903	ev_fork_stop (EV_P_ ev_fork *w) EV_NOEXCEPT
4573	{	4904	{
4574	clear_pending (EV_A_ (W)w);	4905	clear_pending (EV_A_ (W)w);
4575	if (expect_false (!ev_is_active (w)))	4906	if (expect_false (!ev_is_active (w)))
4576	return;	4907	return;
4577		4908
…		…
4590	}	4921	}
4591	#endif	4922	#endif
4592		4923
4593	#if EV_CLEANUP_ENABLE	4924	#if EV_CLEANUP_ENABLE
4594	void	4925	void
4595	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_THROW	4926	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4596	{	4927	{
4597	if (expect_false (ev_is_active (w)))	4928	if (expect_false (ev_is_active (w)))
4598	return;	4929	return;
4599		4930
4600	EV_FREQUENT_CHECK;	4931	EV_FREQUENT_CHECK;
4601		4932
4602	ev_start (EV_A_ (W)w, ++cleanupcnt);	4933	ev_start (EV_A_ (W)w, ++cleanupcnt);
4603	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, EMPTY2);	4934	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, array_needsize_noinit);
4604	cleanups [cleanupcnt - 1] = w;	4935	cleanups [cleanupcnt - 1] = w;
4605		4936
4606	/* cleanup watchers should never keep a refcount on the loop */	4937	/* cleanup watchers should never keep a refcount on the loop */
4607	ev_unref (EV_A);	4938	ev_unref (EV_A);
4608	EV_FREQUENT_CHECK;	4939	EV_FREQUENT_CHECK;
4609	}	4940	}
4610		4941
4611	void	4942	void
4612	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_THROW	4943	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4613	{	4944	{
4614	clear_pending (EV_A_ (W)w);	4945	clear_pending (EV_A_ (W)w);
4615	if (expect_false (!ev_is_active (w)))	4946	if (expect_false (!ev_is_active (w)))
4616	return;	4947	return;
4617		4948
…		…
4631	}	4962	}
4632	#endif	4963	#endif
4633		4964
4634	#if EV_ASYNC_ENABLE	4965	#if EV_ASYNC_ENABLE
4635	void	4966	void
4636	ev_async_start (EV_P_ ev_async *w) EV_THROW	4967	ev_async_start (EV_P_ ev_async *w) EV_NOEXCEPT
4637	{	4968	{
4638	if (expect_false (ev_is_active (w)))	4969	if (expect_false (ev_is_active (w)))
4639	return;	4970	return;
4640		4971
4641	w->sent = 0;	4972	w->sent = 0;
…		…
4643	evpipe_init (EV_A);	4974	evpipe_init (EV_A);
4644		4975
4645	EV_FREQUENT_CHECK;	4976	EV_FREQUENT_CHECK;
4646		4977
4647	ev_start (EV_A_ (W)w, ++asynccnt);	4978	ev_start (EV_A_ (W)w, ++asynccnt);
4648	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, EMPTY2);	4979	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, array_needsize_noinit);
4649	asyncs [asynccnt - 1] = w;	4980	asyncs [asynccnt - 1] = w;
4650		4981
4651	EV_FREQUENT_CHECK;	4982	EV_FREQUENT_CHECK;
4652	}	4983	}
4653		4984
4654	void	4985	void
4655	ev_async_stop (EV_P_ ev_async *w) EV_THROW	4986	ev_async_stop (EV_P_ ev_async *w) EV_NOEXCEPT
4656	{	4987	{
4657	clear_pending (EV_A_ (W)w);	4988	clear_pending (EV_A_ (W)w);
4658	if (expect_false (!ev_is_active (w)))	4989	if (expect_false (!ev_is_active (w)))
4659	return;	4990	return;
4660		4991
…		…
4671		5002
4672	EV_FREQUENT_CHECK;	5003	EV_FREQUENT_CHECK;
4673	}	5004	}
4674		5005
4675	void	5006	void
4676	ev_async_send (EV_P_ ev_async *w) EV_THROW	5007	ev_async_send (EV_P_ ev_async *w) EV_NOEXCEPT
4677	{	5008	{
4678	w->sent = 1;	5009	w->sent = 1;
4679	evpipe_write (EV_A_ &async_pending);	5010	evpipe_write (EV_A_ &async_pending);
4680	}	5011	}
4681	#endif	5012	#endif
…		…
4718		5049
4719	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));	5050	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));
4720	}	5051	}
4721		5052
4722	void	5053	void
4723	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_THROW	5054	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_NOEXCEPT
4724	{	5055	{
4725	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));	5056	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		5057
4733	once->cb = cb;	5058	once->cb = cb;
4734	once->arg = arg;	5059	once->arg = arg;
4735		5060
4736	ev_init (&once->io, once_cb_io);	5061	ev_init (&once->io, once_cb_io);
…		…
4749	}	5074	}
4750		5075
4751	/*****************************************************************************/	5076	/*****************************************************************************/
4752		5077
4753	#if EV_WALK_ENABLE	5078	#if EV_WALK_ENABLE
4754	void ecb_cold	5079	ecb_cold
		5080	void
4755	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_THROW	5081	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_NOEXCEPT
4756	{	5082	{
4757	int i, j;	5083	int i, j;
4758	ev_watcher_list *wl, *wn;	5084	ev_watcher_list *wl, *wn;
4759		5085
4760	if (types & (EV_IO | EV_EMBED))	5086	if (types & (EV_IO | EV_EMBED))

Diff Legend

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