ViewVC Help

View File | Revision Log | Show Annotations | Download File

/cvs/libev/ev.c

Comparing libev/ev.c (file contents):
Revision 1.474 by root, Wed Feb 11 19:20:21 2015 UTC vs.
Revision 1.521 by root, Sat Dec 28 07:47:35 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	*
…		…
115	# else	115	# else
116	# undef EV_USE_EPOLL	116	# undef EV_USE_EPOLL
117	# define EV_USE_EPOLL 0	117	# define EV_USE_EPOLL 0
118	# endif	118	# endif
119		119
		120	# if HAVE_LINUX_AIO_ABI_H
		121	# ifndef EV_USE_LINUXAIO
		122	# define EV_USE_LINUXAIO 0 /* was: EV_FEATURE_BACKENDS, always off by default */
		123	# endif
		124	# else
		125	# undef EV_USE_LINUXAIO
		126	# define EV_USE_LINUXAIO 0
		127	# endif
		128
		129	# if HAVE_LINUX_FS_H && HAVE_SYS_TIMERFD_H && HAVE_KERNEL_RWF_T
		130	# ifndef EV_USE_IOURING
		131	# define EV_USE_IOURING EV_FEATURE_BACKENDS
		132	# endif
		133	# else
		134	# undef EV_USE_IOURING
		135	# define EV_USE_IOURING 0
		136	# endif
		137
120	# if HAVE_KQUEUE && HAVE_SYS_EVENT_H	138	# if HAVE_KQUEUE && HAVE_SYS_EVENT_H
121	# ifndef EV_USE_KQUEUE	139	# ifndef EV_USE_KQUEUE
122	# define EV_USE_KQUEUE EV_FEATURE_BACKENDS	140	# define EV_USE_KQUEUE EV_FEATURE_BACKENDS
123	# endif	141	# endif
124	# else	142	# else
…		…
159	# endif	177	# endif
160	# else	178	# else
161	# undef EV_USE_EVENTFD	179	# undef EV_USE_EVENTFD
162	# define EV_USE_EVENTFD 0	180	# define EV_USE_EVENTFD 0
163	# endif	181	# endif
164		182
		183	# if HAVE_SYS_TIMERFD_H
		184	# ifndef EV_USE_TIMERFD
		185	# define EV_USE_TIMERFD EV_FEATURE_OS
		186	# endif
		187	# else
		188	# undef EV_USE_TIMERFD
		189	# define EV_USE_TIMERFD 0
165	#endif	190	# endif
		191
		192	#endif
		193
		194	/* OS X, in its infinite idiocy, actually HARDCODES
		195	* a limit of 1024 into their select. Where people have brains,
		196	* OS X engineers apparently have a vacuum. Or maybe they were
		197	* ordered to have a vacuum, or they do anything for money.
		198	* This might help. Or not.
		199	* Note that this must be defined early, as other include files
		200	* will rely on this define as well.
		201	*/
		202	#define _DARWIN_UNLIMITED_SELECT 1
166		203
167	#include <stdlib.h>	204	#include <stdlib.h>
168	#include <string.h>	205	#include <string.h>
169	#include <fcntl.h>	206	#include <fcntl.h>
170	#include <stddef.h>	207	#include <stddef.h>
…		…
208	# ifndef EV_SELECT_IS_WINSOCKET	245	# ifndef EV_SELECT_IS_WINSOCKET
209	# define EV_SELECT_IS_WINSOCKET 1	246	# define EV_SELECT_IS_WINSOCKET 1
210	# endif	247	# endif
211	# undef EV_AVOID_STDIO	248	# undef EV_AVOID_STDIO
212	#endif	249	#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		250
222	/* this block tries to deduce configuration from header-defined symbols and defaults */	251	/* this block tries to deduce configuration from header-defined symbols and defaults */
223		252
224	/* try to deduce the maximum number of signals on this platform */	253	/* try to deduce the maximum number of signals on this platform */
225	#if defined EV_NSIG	254	#if defined EV_NSIG
…		…
313		342
314	#ifndef EV_USE_PORT	343	#ifndef EV_USE_PORT
315	# define EV_USE_PORT 0	344	# define EV_USE_PORT 0
316	#endif	345	#endif
317		346
		347	#ifndef EV_USE_LINUXAIO
		348	# if __linux /* libev currently assumes linux/aio_abi.h is always available on linux */
		349	# define EV_USE_LINUXAIO 0 /* was: 1, always off by default */
		350	# else
		351	# define EV_USE_LINUXAIO 0
		352	# endif
		353	#endif
		354
		355	#ifndef EV_USE_IOURING
		356	# if __linux /* later checks might disable again */
		357	# define EV_USE_IOURING 1
		358	# else
		359	# define EV_USE_IOURING 0
		360	# endif
		361	#endif
		362
318	#ifndef EV_USE_INOTIFY	363	#ifndef EV_USE_INOTIFY
319	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))	364	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))
320	# define EV_USE_INOTIFY EV_FEATURE_OS	365	# define EV_USE_INOTIFY EV_FEATURE_OS
321	# else	366	# else
322	# define EV_USE_INOTIFY 0	367	# define EV_USE_INOTIFY 0
…		…
345	# else	390	# else
346	# define EV_USE_SIGNALFD 0	391	# define EV_USE_SIGNALFD 0
347	# endif	392	# endif
348	#endif	393	#endif
349		394
		395	#ifndef EV_USE_TIMERFD
		396	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 8))
		397	# define EV_USE_TIMERFD EV_FEATURE_OS
		398	# else
		399	# define EV_USE_TIMERFD 0
		400	# endif
		401	#endif
		402
350	#if 0 /* debugging */	403	#if 0 /* debugging */
351	# define EV_VERIFY 3	404	# define EV_VERIFY 3
352	# define EV_USE_4HEAP 1	405	# define EV_USE_4HEAP 1
353	# define EV_HEAP_CACHE_AT 1	406	# define EV_HEAP_CACHE_AT 1
354	#endif	407	#endif
…		…
363		416
364	#ifndef EV_HEAP_CACHE_AT	417	#ifndef EV_HEAP_CACHE_AT
365	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA	418	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA
366	#endif	419	#endif
367		420
368	#ifdef ANDROID	421	#ifdef __ANDROID__
369	/* supposedly, android doesn't typedef fd_mask */	422	/* supposedly, android doesn't typedef fd_mask */
370	# undef EV_USE_SELECT	423	# undef EV_USE_SELECT
371	# define EV_USE_SELECT 0	424	# define EV_USE_SELECT 0
372	/* supposedly, we need to include syscall.h, not sys/syscall.h, so just disable */	425	/* supposedly, we need to include syscall.h, not sys/syscall.h, so just disable */
373	# undef EV_USE_CLOCK_SYSCALL	426	# undef EV_USE_CLOCK_SYSCALL
…		…
387	# include <sys/syscall.h>	440	# include <sys/syscall.h>
388	# ifdef SYS_clock_gettime	441	# ifdef SYS_clock_gettime
389	# define clock_gettime(id, ts) syscall (SYS_clock_gettime, (id), (ts))	442	# define clock_gettime(id, ts) syscall (SYS_clock_gettime, (id), (ts))
390	# undef EV_USE_MONOTONIC	443	# undef EV_USE_MONOTONIC
391	# define EV_USE_MONOTONIC 1	444	# define EV_USE_MONOTONIC 1
		445	# define EV_NEED_SYSCALL 1
392	# else	446	# else
393	# undef EV_USE_CLOCK_SYSCALL	447	# undef EV_USE_CLOCK_SYSCALL
394	# define EV_USE_CLOCK_SYSCALL 0	448	# define EV_USE_CLOCK_SYSCALL 0
395	# endif	449	# endif
396	#endif	450	#endif
…		…
410	#if !EV_STAT_ENABLE	464	#if !EV_STAT_ENABLE
411	# undef EV_USE_INOTIFY	465	# undef EV_USE_INOTIFY
412	# define EV_USE_INOTIFY 0	466	# define EV_USE_INOTIFY 0
413	#endif	467	#endif
414		468
		469	#if __linux && EV_USE_IOURING
		470	# include <linux/version.h>
		471	# if LINUX_VERSION_CODE < KERNEL_VERSION(4,14,0)
		472	# undef EV_USE_IOURING
		473	# define EV_USE_IOURING 0
		474	# endif
		475	#endif
		476
415	#if !EV_USE_NANOSLEEP	477	#if !EV_USE_NANOSLEEP
416	/* hp-ux has it in sys/time.h, which we unconditionally include above */	478	/* hp-ux has it in sys/time.h, which we unconditionally include above */
417	# if !defined _WIN32 && !defined __hpux	479	# if !defined _WIN32 && !defined __hpux
418	# include <sys/select.h>	480	# include <sys/select.h>
		481	# endif
		482	#endif
		483
		484	#if EV_USE_LINUXAIO
		485	# include <sys/syscall.h>
		486	# if SYS_io_getevents && EV_USE_EPOLL /* linuxaio backend requires epoll backend */
		487	# define EV_NEED_SYSCALL 1
		488	# else
		489	# undef EV_USE_LINUXAIO
		490	# define EV_USE_LINUXAIO 0
		491	# endif
		492	#endif
		493
		494	#if EV_USE_IOURING
		495	# include <sys/syscall.h>
		496	# if !SYS_io_uring_setup && __linux && !__alpha
		497	# define SYS_io_uring_setup 425
		498	# define SYS_io_uring_enter 426
		499	# define SYS_io_uring_wregister 427
		500	# endif
		501	# if SYS_io_uring_setup && EV_USE_EPOLL /* iouring backend requires epoll backend */
		502	# define EV_NEED_SYSCALL 1
		503	# else
		504	# undef EV_USE_IOURING
		505	# define EV_USE_IOURING 0
419	# endif	506	# endif
420	#endif	507	#endif
421		508
422	#if EV_USE_INOTIFY	509	#if EV_USE_INOTIFY
423	# include <sys/statfs.h>	510	# include <sys/statfs.h>
…		…
428	# define EV_USE_INOTIFY 0	515	# define EV_USE_INOTIFY 0
429	# endif	516	# endif
430	#endif	517	#endif
431		518
432	#if EV_USE_EVENTFD	519	#if EV_USE_EVENTFD
433	/* our minimum requirement is glibc 2.7 which has the stub, but not the header */	520	/* our minimum requirement is glibc 2.7 which has the stub, but not the full header */
434	# include <stdint.h>	521	# include <stdint.h>
435	# ifndef EFD_NONBLOCK	522	# ifndef EFD_NONBLOCK
436	# define EFD_NONBLOCK O_NONBLOCK	523	# define EFD_NONBLOCK O_NONBLOCK
437	# endif	524	# endif
438	# ifndef EFD_CLOEXEC	525	# ifndef EFD_CLOEXEC
…		…
444	# endif	531	# endif
445	EV_CPP(extern "C") int (eventfd) (unsigned int initval, int flags);	532	EV_CPP(extern "C") int (eventfd) (unsigned int initval, int flags);
446	#endif	533	#endif
447		534
448	#if EV_USE_SIGNALFD	535	#if EV_USE_SIGNALFD
449	/* our minimum requirement is glibc 2.7 which has the stub, but not the header */	536	/* our minimum requirement is glibc 2.7 which has the stub, but not the full header */
450	# include <stdint.h>	537	# include <stdint.h>
451	# ifndef SFD_NONBLOCK	538	# ifndef SFD_NONBLOCK
452	# define SFD_NONBLOCK O_NONBLOCK	539	# define SFD_NONBLOCK O_NONBLOCK
453	# endif	540	# endif
454	# ifndef SFD_CLOEXEC	541	# ifndef SFD_CLOEXEC
…		…
456	# define SFD_CLOEXEC O_CLOEXEC	543	# define SFD_CLOEXEC O_CLOEXEC
457	# else	544	# else
458	# define SFD_CLOEXEC 02000000	545	# define SFD_CLOEXEC 02000000
459	# endif	546	# endif
460	# endif	547	# endif
461	EV_CPP (extern "C") int signalfd (int fd, const sigset_t *mask, int flags);	548	EV_CPP (extern "C") int (signalfd) (int fd, const sigset_t *mask, int flags);
462		549
463	struct signalfd_siginfo	550	struct signalfd_siginfo
464	{	551	{
465	uint32_t ssi_signo;	552	uint32_t ssi_signo;
466	char pad[128 - sizeof (uint32_t)];	553	char pad[128 - sizeof (uint32_t)];
467	};	554	};
468	#endif	555	#endif
469		556
470	/**/	557	/* for timerfd, libev core requires TFD_TIMER_CANCEL_ON_SET &c */
		558	#if EV_USE_TIMERFD
		559	# include <sys/timerfd.h>
		560	/* timerfd is only used for periodics */
		561	# if !(defined (TFD_TIMER_CANCEL_ON_SET) && defined (TFD_CLOEXEC) && defined (TFD_NONBLOCK)) || !EV_PERIODIC_ENABLE
		562	# undef EV_USE_TIMERFD
		563	# define EV_USE_TIMERFD 0
		564	# endif
		565	#endif
		566
		567	/*****************************************************************************/
471		568
472	#if EV_VERIFY >= 3	569	#if EV_VERIFY >= 3
473	# define EV_FREQUENT_CHECK ev_verify (EV_A)	570	# define EV_FREQUENT_CHECK ev_verify (EV_A)
474	#else	571	#else
475	# define EV_FREQUENT_CHECK do { } while (0)	572	# define EV_FREQUENT_CHECK do { } while (0)
…		…
480	* This value is good at least till the year 4000.	577	* This value is good at least till the year 4000.
481	*/	578	*/
482	#define MIN_INTERVAL 0.0001220703125 /* 1/2**13, good till 4000 */	579	#define MIN_INTERVAL 0.0001220703125 /* 1/2**13, good till 4000 */
483	/*#define MIN_INTERVAL 0.00000095367431640625 /* 1/2**20, good till 2200 */	580	/*#define MIN_INTERVAL 0.00000095367431640625 /* 1/2**20, good till 2200 */
484		581
485	#define MIN_TIMEJUMP 1. /* minimum timejump that gets detected (if monotonic clock available) */	582	#define MIN_TIMEJUMP 1. /* minimum timejump that gets detected (if monotonic clock available) */
486	#define MAX_BLOCKTIME 59.743 /* never wait longer than this time (to detect time jumps) */	583	#define MAX_BLOCKTIME 59.743 /* never wait longer than this time (to detect time jumps) */
487		584
		585	/* find a portable timestamp that is "always" in the future but fits into time_t.
		586	* this is quite hard, and we are mostly guessing - we handle 32 bit signed/unsigned time_t,
		587	* and sizes larger than 32 bit, and maybe the unlikely floating point time_t */
		588	#define EV_TSTAMP_HUGE \
		589	(sizeof (time_t) >= 8 ? 10000000000000. \
		590	: 0 < (time_t)4294967295 ? 4294967295. \
		591	: 2147483647.) \
		592
		593	#ifndef EV_TS_CONST
		594	# define EV_TS_CONST(nv) nv
		595	# define EV_TS_TO_MSEC(a) a * 1e3 + 0.9999
		596	# define EV_TS_FROM_USEC(us) us * 1e-6
488	#define EV_TV_SET(tv,t) do { tv.tv_sec = (long)t; tv.tv_usec = (long)((t - tv.tv_sec) * 1e6); } while (0)	597	# define EV_TV_SET(tv,t) do { tv.tv_sec = (long)t; tv.tv_usec = (long)((t - tv.tv_sec) * 1e6); } while (0)
489	#define EV_TS_SET(ts,t) do { ts.tv_sec = (long)t; ts.tv_nsec = (long)((t - ts.tv_sec) * 1e9); } while (0)	598	# define EV_TS_SET(ts,t) do { ts.tv_sec = (long)t; ts.tv_nsec = (long)((t - ts.tv_sec) * 1e9); } while (0)
		599	# define EV_TV_GET(tv) ((tv).tv_sec + (tv).tv_usec * 1e-6)
		600	# define EV_TS_GET(ts) ((ts).tv_sec + (ts).tv_nsec * 1e-9)
		601	#endif
490		602
491	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */	603	/* the following is ecb.h embedded into libev - use update_ev_c to update from an external copy */
492	/* ECB.H BEGIN */	604	/* ECB.H BEGIN */
493	/*	605	/*
494	* libecb - http://software.schmorp.de/pkg/libecb	606	* libecb - http://software.schmorp.de/pkg/libecb
…		…
532		644
533	#ifndef ECB_H	645	#ifndef ECB_H
534	#define ECB_H	646	#define ECB_H
535		647
536	/* 16 bits major, 16 bits minor */	648	/* 16 bits major, 16 bits minor */
537	#define ECB_VERSION 0x00010004	649	#define ECB_VERSION 0x00010006
538		650
539	#ifdef _WIN32	651	#ifdef _WIN32
540	typedef signed char int8_t;	652	typedef signed char int8_t;
541	typedef unsigned char uint8_t;	653	typedef unsigned char uint8_t;
542	typedef signed short int16_t;	654	typedef signed short int16_t;
…		…
559	typedef uint32_t uintptr_t;	671	typedef uint32_t uintptr_t;
560	typedef int32_t intptr_t;	672	typedef int32_t intptr_t;
561	#endif	673	#endif
562	#else	674	#else
563	#include <inttypes.h>	675	#include <inttypes.h>
564	#if UINTMAX_MAX > 0xffffffffU	676	#if (defined INTPTR_MAX ? INTPTR_MAX : ULONG_MAX) > 0xffffffffU
565	#define ECB_PTRSIZE 8	677	#define ECB_PTRSIZE 8
566	#else	678	#else
567	#define ECB_PTRSIZE 4	679	#define ECB_PTRSIZE 4
568	#endif	680	#endif
569	#endif	681	#endif
570		682
		683	#define ECB_GCC_AMD64 (__amd64 || __amd64__ || __x86_64 || __x86_64__)
		684	#define ECB_MSVC_AMD64 (_M_AMD64 || _M_X64)
		685
571	/* work around x32 idiocy by defining proper macros */	686	/* work around x32 idiocy by defining proper macros */
572	#if __amd64 || __x86_64 || _M_AMD64 || _M_X64	687	#if ECB_GCC_AMD64 || ECB_MSVC_AMD64
573	#if _ILP32	688	#if _ILP32
574	#define ECB_AMD64_X32 1	689	#define ECB_AMD64_X32 1
575	#else	690	#else
576	#define ECB_AMD64 1	691	#define ECB_AMD64 1
577	#endif	692	#endif
…		…
604	#define ECB_CLANG_EXTENSION(x) 0	719	#define ECB_CLANG_EXTENSION(x) 0
605	#endif	720	#endif
606		721
607	#define ECB_CPP (__cplusplus+0)	722	#define ECB_CPP (__cplusplus+0)
608	#define ECB_CPP11 (__cplusplus >= 201103L)	723	#define ECB_CPP11 (__cplusplus >= 201103L)
		724	#define ECB_CPP14 (__cplusplus >= 201402L)
		725	#define ECB_CPP17 (__cplusplus >= 201703L)
609		726
610	#if ECB_CPP	727	#if ECB_CPP
611	#define ECB_C 0	728	#define ECB_C 0
612	#define ECB_STDC_VERSION 0	729	#define ECB_STDC_VERSION 0
613	#else	730	#else
…		…
615	#define ECB_STDC_VERSION __STDC_VERSION__	732	#define ECB_STDC_VERSION __STDC_VERSION__
616	#endif	733	#endif
617		734
618	#define ECB_C99 (ECB_STDC_VERSION >= 199901L)	735	#define ECB_C99 (ECB_STDC_VERSION >= 199901L)
619	#define ECB_C11 (ECB_STDC_VERSION >= 201112L)	736	#define ECB_C11 (ECB_STDC_VERSION >= 201112L)
		737	#define ECB_C17 (ECB_STDC_VERSION >= 201710L)
620		738
621	#if ECB_CPP	739	#if ECB_CPP
622	#define ECB_EXTERN_C extern "C"	740	#define ECB_EXTERN_C extern "C"
623	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {	741	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {
624	#define ECB_EXTERN_C_END }	742	#define ECB_EXTERN_C_END }
…		…
639		757
640	#if ECB_NO_SMP	758	#if ECB_NO_SMP
641	#define ECB_MEMORY_FENCE do { } while (0)	759	#define ECB_MEMORY_FENCE do { } while (0)
642	#endif	760	#endif
643		761
		762	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/compiler_ref/compiler_builtins.html */
		763	#if __xlC__ && ECB_CPP
		764	#include <builtins.h>
		765	#endif
		766
		767	#if 1400 <= _MSC_VER
		768	#include <intrin.h> /* fence functions _ReadBarrier, also bit search functions _BitScanReverse */
		769	#endif
		770
644	#ifndef ECB_MEMORY_FENCE	771	#ifndef ECB_MEMORY_FENCE
645	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	772	#if ECB_GCC_VERSION(2,5) || defined __INTEL_COMPILER || (__llvm__ && __GNUC__) || __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
		773	#define ECB_MEMORY_FENCE_RELAXED __asm__ __volatile__ ("" : : : "memory")
646	#if __i386 || __i386__	774	#if __i386 || __i386__
647	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")	775	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("lock; orb $0, -1(%%esp)" : : : "memory")
648	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")	776	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
649	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	777	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
650	#elif __amd64 || __amd64__ || __x86_64 || __x86_64__	778	#elif ECB_GCC_AMD64
651	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")	779	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")
652	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")	780	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
653	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	781	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
654	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__	782	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__
655	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")	783	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory")
		784	#elif defined __ARM_ARCH_2__ \
		785	|| defined __ARM_ARCH_3__ || defined __ARM_ARCH_3M__ \
		786	|| defined __ARM_ARCH_4__ || defined __ARM_ARCH_4T__ \
		787	|| defined __ARM_ARCH_5__ || defined __ARM_ARCH_5E__ \
		788	|| defined __ARM_ARCH_5T__ || defined __ARM_ARCH_5TE__ \
		789	|| defined __ARM_ARCH_5TEJ__
		790	/* should not need any, unless running old code on newer cpu - arm doesn't support that */
656	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \	791	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \
657	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__	792	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__ \
		793	|| defined __ARM_ARCH_6T2__
658	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")	794	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mcr p15,0,%0,c7,c10,5" : : "r" (0) : "memory")
659	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \	795	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \
660	|| defined __ARM_ARCH_7M__ || defined __ARM_ARCH_7R__	796	|| defined __ARM_ARCH_7R__ || defined __ARM_ARCH_7M__
661	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")	797	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")
662	#elif __aarch64__	798	#elif __aarch64__
663	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb ish" : : : "memory")	799	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb ish" : : : "memory")
664	#elif (__sparc || __sparc__) && !__sparcv8	800	#elif (__sparc || __sparc__) && !(__sparc_v8__ || defined __sparcv8)
665	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")	801	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad | #StoreStore | #StoreLoad" : : : "memory")
666	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")	802	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")
667	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")	803	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")
668	#elif defined __s390__ || defined __s390x__	804	#elif defined __s390__ || defined __s390x__
669	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")	805	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")
…		…
692	#if ECB_GCC_VERSION(4,7)	828	#if ECB_GCC_VERSION(4,7)
693	/* see comment below (stdatomic.h) about the C11 memory model. */	829	/* see comment below (stdatomic.h) about the C11 memory model. */
694	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)	830	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)
695	#define ECB_MEMORY_FENCE_ACQUIRE __atomic_thread_fence (__ATOMIC_ACQUIRE)	831	#define ECB_MEMORY_FENCE_ACQUIRE __atomic_thread_fence (__ATOMIC_ACQUIRE)
696	#define ECB_MEMORY_FENCE_RELEASE __atomic_thread_fence (__ATOMIC_RELEASE)	832	#define ECB_MEMORY_FENCE_RELEASE __atomic_thread_fence (__ATOMIC_RELEASE)
		833	#define ECB_MEMORY_FENCE_RELAXED __atomic_thread_fence (__ATOMIC_RELAXED)
697		834
698	#elif ECB_CLANG_EXTENSION(c_atomic)	835	#elif ECB_CLANG_EXTENSION(c_atomic)
699	/* see comment below (stdatomic.h) about the C11 memory model. */	836	/* see comment below (stdatomic.h) about the C11 memory model. */
700	#define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)	837	#define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)
701	#define ECB_MEMORY_FENCE_ACQUIRE __c11_atomic_thread_fence (__ATOMIC_ACQUIRE)	838	#define ECB_MEMORY_FENCE_ACQUIRE __c11_atomic_thread_fence (__ATOMIC_ACQUIRE)
702	#define ECB_MEMORY_FENCE_RELEASE __c11_atomic_thread_fence (__ATOMIC_RELEASE)	839	#define ECB_MEMORY_FENCE_RELEASE __c11_atomic_thread_fence (__ATOMIC_RELEASE)
		840	#define ECB_MEMORY_FENCE_RELAXED __c11_atomic_thread_fence (__ATOMIC_RELAXED)
703		841
704	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__	842	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__
705	#define ECB_MEMORY_FENCE __sync_synchronize ()	843	#define ECB_MEMORY_FENCE __sync_synchronize ()
706	#elif _MSC_VER >= 1500 /* VC++ 2008 */	844	#elif _MSC_VER >= 1500 /* VC++ 2008 */
707	/* apparently, microsoft broke all the memory barrier stuff in Visual Studio 2008... */	845	/* apparently, microsoft broke all the memory barrier stuff in Visual Studio 2008... */
…		…
717	#elif defined _WIN32	855	#elif defined _WIN32
718	#include <WinNT.h>	856	#include <WinNT.h>
719	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */	857	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */
720	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	858	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
721	#include <mbarrier.h>	859	#include <mbarrier.h>
722	#define ECB_MEMORY_FENCE __machine_rw_barrier ()	860	#define ECB_MEMORY_FENCE __machine_rw_barrier ()
723	#define ECB_MEMORY_FENCE_ACQUIRE __machine_r_barrier ()	861	#define ECB_MEMORY_FENCE_ACQUIRE __machine_acq_barrier ()
724	#define ECB_MEMORY_FENCE_RELEASE __machine_w_barrier ()	862	#define ECB_MEMORY_FENCE_RELEASE __machine_rel_barrier ()
		863	#define ECB_MEMORY_FENCE_RELAXED __compiler_barrier ()
725	#elif __xlC__	864	#elif __xlC__
726	#define ECB_MEMORY_FENCE __sync ()	865	#define ECB_MEMORY_FENCE __sync ()
727	#endif	866	#endif
728	#endif	867	#endif
729		868
730	#ifndef ECB_MEMORY_FENCE	869	#ifndef ECB_MEMORY_FENCE
731	#if ECB_C11 && !defined __STDC_NO_ATOMICS__	870	#if ECB_C11 && !defined __STDC_NO_ATOMICS__
732	/* we assume that these memory fences work on all variables/all memory accesses, */	871	/* we assume that these memory fences work on all variables/all memory accesses, */
733	/* not just C11 atomics and atomic accesses */	872	/* not just C11 atomics and atomic accesses */
734	#include <stdatomic.h>	873	#include <stdatomic.h>
735	/* Unfortunately, neither gcc 4.7 nor clang 3.1 generate any instructions for */
736	/* any fence other than seq_cst, which isn't very efficient for us. */
737	/* Why that is, we don't know - either the C11 memory model is quite useless */
738	/* for most usages, or gcc and clang have a bug */
739	/* I *currently* lean towards the latter, and inefficiently implement */
740	/* all three of ecb's fences as a seq_cst fence */
741	/* Update, gcc-4.8 generates mfence for all c++ fences, but nothing */
742	/* for all __atomic_thread_fence's except seq_cst */
743	#define ECB_MEMORY_FENCE atomic_thread_fence (memory_order_seq_cst)	874	#define ECB_MEMORY_FENCE atomic_thread_fence (memory_order_seq_cst)
		875	#define ECB_MEMORY_FENCE_ACQUIRE atomic_thread_fence (memory_order_acquire)
		876	#define ECB_MEMORY_FENCE_RELEASE atomic_thread_fence (memory_order_release)
744	#endif	877	#endif
745	#endif	878	#endif
746		879
747	#ifndef ECB_MEMORY_FENCE	880	#ifndef ECB_MEMORY_FENCE
748	#if !ECB_AVOID_PTHREADS	881	#if !ECB_AVOID_PTHREADS
…		…
768		901
769	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE	902	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE
770	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	903	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
771	#endif	904	#endif
772		905
		906	#if !defined ECB_MEMORY_FENCE_RELAXED && defined ECB_MEMORY_FENCE
		907	#define ECB_MEMORY_FENCE_RELAXED ECB_MEMORY_FENCE /* very heavy-handed */
		908	#endif
		909
773	/*****************************************************************************/	910	/*****************************************************************************/
774		911
775	#if ECB_CPP	912	#if ECB_CPP
776	#define ecb_inline static inline	913	#define ecb_inline static inline
777	#elif ECB_GCC_VERSION(2,5)	914	#elif ECB_GCC_VERSION(2,5)
…		…
794		931
795	#define ECB_CONCAT_(a, b) a ## b	932	#define ECB_CONCAT_(a, b) a ## b
796	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)	933	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)
797	#define ECB_STRINGIFY_(a) # a	934	#define ECB_STRINGIFY_(a) # a
798	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)	935	#define ECB_STRINGIFY(a) ECB_STRINGIFY_(a)
		936	#define ECB_STRINGIFY_EXPR(expr) ((expr), ECB_STRINGIFY_ (expr))
799		937
800	#define ecb_function_ ecb_inline	938	#define ecb_function_ ecb_inline
801		939
802	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_VERSION(2,8)	940	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_VERSION(2,8)
803	#define ecb_attribute(attrlist) __attribute__ (attrlist)	941	#define ecb_attribute(attrlist) __attribute__ (attrlist)
…		…
840	#define ecb_deprecated __declspec (deprecated)	978	#define ecb_deprecated __declspec (deprecated)
841	#else	979	#else
842	#define ecb_deprecated ecb_attribute ((__deprecated__))	980	#define ecb_deprecated ecb_attribute ((__deprecated__))
843	#endif	981	#endif
844		982
		983	#if _MSC_VER >= 1500
		984	#define ecb_deprecated_message(msg) __declspec (deprecated (msg))
		985	#elif ECB_GCC_VERSION(4,5)
		986	#define ecb_deprecated_message(msg) ecb_attribute ((__deprecated__ (msg))
		987	#else
		988	#define ecb_deprecated_message(msg) ecb_deprecated
		989	#endif
		990
		991	#if _MSC_VER >= 1400
		992	#define ecb_noinline __declspec (noinline)
		993	#else
845	#define ecb_noinline ecb_attribute ((__noinline__))	994	#define ecb_noinline ecb_attribute ((__noinline__))
		995	#endif
		996
846	#define ecb_unused ecb_attribute ((__unused__))	997	#define ecb_unused ecb_attribute ((__unused__))
847	#define ecb_const ecb_attribute ((__const__))	998	#define ecb_const ecb_attribute ((__const__))
848	#define ecb_pure ecb_attribute ((__pure__))	999	#define ecb_pure ecb_attribute ((__pure__))
849		1000
850	/* TODO http://msdn.microsoft.com/en-us/library/k6ktzx3s.aspx __declspec(noreturn) */
851	#if ECB_C11 || __IBMC_NORETURN	1001	#if ECB_C11 || __IBMC_NORETURN
852	/* http://pic.dhe.ibm.com/infocenter/compbg/v121v141/topic/com.ibm.xlcpp121.bg.doc/language_ref/noreturn.html */	1002	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/language_ref/noreturn.html */
853	#define ecb_noreturn _Noreturn	1003	#define ecb_noreturn _Noreturn
		1004	#elif ECB_CPP11
		1005	#define ecb_noreturn [[noreturn]]
		1006	#elif _MSC_VER >= 1200
		1007	/* http://msdn.microsoft.com/en-us/library/k6ktzx3s.aspx */
		1008	#define ecb_noreturn __declspec (noreturn)
854	#else	1009	#else
855	#define ecb_noreturn ecb_attribute ((__noreturn__))	1010	#define ecb_noreturn ecb_attribute ((__noreturn__))
856	#endif	1011	#endif
857		1012
858	#if ECB_GCC_VERSION(4,3)	1013	#if ECB_GCC_VERSION(4,3)
…		…
889	#else	1044	#else
890	ecb_function_ ecb_const int ecb_ctz32 (uint32_t x);	1045	ecb_function_ ecb_const int ecb_ctz32 (uint32_t x);
891	ecb_function_ ecb_const int	1046	ecb_function_ ecb_const int
892	ecb_ctz32 (uint32_t x)	1047	ecb_ctz32 (uint32_t x)
893	{	1048	{
		1049	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		1050	unsigned long r;
		1051	_BitScanForward (&r, x);
		1052	return (int)r;
		1053	#else
894	int r = 0;	1054	int r = 0;
895		1055
896	x &= ~x + 1; /* this isolates the lowest bit */	1056	x &= ~x + 1; /* this isolates the lowest bit */
897		1057
898	#if ECB_branchless_on_i386	1058	#if ECB_branchless_on_i386
…		…
908	if (x & 0xff00ff00) r += 8;	1068	if (x & 0xff00ff00) r += 8;
909	if (x & 0xffff0000) r += 16;	1069	if (x & 0xffff0000) r += 16;
910	#endif	1070	#endif
911		1071
912	return r;	1072	return r;
		1073	#endif
913	}	1074	}
914		1075
915	ecb_function_ ecb_const int ecb_ctz64 (uint64_t x);	1076	ecb_function_ ecb_const int ecb_ctz64 (uint64_t x);
916	ecb_function_ ecb_const int	1077	ecb_function_ ecb_const int
917	ecb_ctz64 (uint64_t x)	1078	ecb_ctz64 (uint64_t x)
918	{	1079	{
		1080	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1081	unsigned long r;
		1082	_BitScanForward64 (&r, x);
		1083	return (int)r;
		1084	#else
919	int shift = x & 0xffffffffU ? 0 : 32;	1085	int shift = x & 0xffffffff ? 0 : 32;
920	return ecb_ctz32 (x >> shift) + shift;	1086	return ecb_ctz32 (x >> shift) + shift;
		1087	#endif
921	}	1088	}
922		1089
923	ecb_function_ ecb_const int ecb_popcount32 (uint32_t x);	1090	ecb_function_ ecb_const int ecb_popcount32 (uint32_t x);
924	ecb_function_ ecb_const int	1091	ecb_function_ ecb_const int
925	ecb_popcount32 (uint32_t x)	1092	ecb_popcount32 (uint32_t x)
…		…
933	}	1100	}
934		1101
935	ecb_function_ ecb_const int ecb_ld32 (uint32_t x);	1102	ecb_function_ ecb_const int ecb_ld32 (uint32_t x);
936	ecb_function_ ecb_const int ecb_ld32 (uint32_t x)	1103	ecb_function_ ecb_const int ecb_ld32 (uint32_t x)
937	{	1104	{
		1105	#if 1400 <= _MSC_VER && (_M_IX86 || _M_X64 || _M_IA64 || _M_ARM)
		1106	unsigned long r;
		1107	_BitScanReverse (&r, x);
		1108	return (int)r;
		1109	#else
938	int r = 0;	1110	int r = 0;
939		1111
940	if (x >> 16) { x >>= 16; r += 16; }	1112	if (x >> 16) { x >>= 16; r += 16; }
941	if (x >> 8) { x >>= 8; r += 8; }	1113	if (x >> 8) { x >>= 8; r += 8; }
942	if (x >> 4) { x >>= 4; r += 4; }	1114	if (x >> 4) { x >>= 4; r += 4; }
943	if (x >> 2) { x >>= 2; r += 2; }	1115	if (x >> 2) { x >>= 2; r += 2; }
944	if (x >> 1) { r += 1; }	1116	if (x >> 1) { r += 1; }
945		1117
946	return r;	1118	return r;
		1119	#endif
947	}	1120	}
948		1121
949	ecb_function_ ecb_const int ecb_ld64 (uint64_t x);	1122	ecb_function_ ecb_const int ecb_ld64 (uint64_t x);
950	ecb_function_ ecb_const int ecb_ld64 (uint64_t x)	1123	ecb_function_ ecb_const int ecb_ld64 (uint64_t x)
951	{	1124	{
		1125	#if 1400 <= _MSC_VER && (_M_X64 || _M_IA64 || _M_ARM)
		1126	unsigned long r;
		1127	_BitScanReverse64 (&r, x);
		1128	return (int)r;
		1129	#else
952	int r = 0;	1130	int r = 0;
953		1131
954	if (x >> 32) { x >>= 32; r += 32; }	1132	if (x >> 32) { x >>= 32; r += 32; }
955		1133
956	return r + ecb_ld32 (x);	1134	return r + ecb_ld32 (x);
		1135	#endif
957	}	1136	}
958	#endif	1137	#endif
959		1138
960	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x);	1139	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x);
961	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x) { return !(x & (x - 1)); }	1140	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x) { return !(x & (x - 1)); }
…		…
1018	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }	1197	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }
1019	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }	1198	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }
1020	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }	1199	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }
1021		1200
1022	#if ECB_GCC_VERSION(4,3) || (ECB_CLANG_BUILTIN(__builtin_bswap32) && ECB_CLANG_BUILTIN(__builtin_bswap64))	1201	#if ECB_GCC_VERSION(4,3) || (ECB_CLANG_BUILTIN(__builtin_bswap32) && ECB_CLANG_BUILTIN(__builtin_bswap64))
		1202	#if ECB_GCC_VERSION(4,8) || ECB_CLANG_BUILTIN(__builtin_bswap16)
		1203	#define ecb_bswap16(x) __builtin_bswap16 (x)
		1204	#else
1023	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)	1205	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)
		1206	#endif
1024	#define ecb_bswap32(x) __builtin_bswap32 (x)	1207	#define ecb_bswap32(x) __builtin_bswap32 (x)
1025	#define ecb_bswap64(x) __builtin_bswap64 (x)	1208	#define ecb_bswap64(x) __builtin_bswap64 (x)
		1209	#elif _MSC_VER
		1210	#include <stdlib.h>
		1211	#define ecb_bswap16(x) ((uint16_t)_byteswap_ushort ((uint16_t)(x)))
		1212	#define ecb_bswap32(x) ((uint32_t)_byteswap_ulong ((uint32_t)(x)))
		1213	#define ecb_bswap64(x) ((uint64_t)_byteswap_uint64 ((uint64_t)(x)))
1026	#else	1214	#else
1027	ecb_function_ ecb_const uint16_t ecb_bswap16 (uint16_t x);	1215	ecb_function_ ecb_const uint16_t ecb_bswap16 (uint16_t x);
1028	ecb_function_ ecb_const uint16_t	1216	ecb_function_ ecb_const uint16_t
1029	ecb_bswap16 (uint16_t x)	1217	ecb_bswap16 (uint16_t x)
1030	{	1218	{
…		…
1055	#endif	1243	#endif
1056		1244
1057	/* try to tell the compiler that some condition is definitely true */	1245	/* try to tell the compiler that some condition is definitely true */
1058	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0	1246	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0
1059		1247
1060	ecb_inline ecb_const unsigned char ecb_byteorder_helper (void);	1248	ecb_inline ecb_const uint32_t ecb_byteorder_helper (void);
1061	ecb_inline ecb_const unsigned char	1249	ecb_inline ecb_const uint32_t
1062	ecb_byteorder_helper (void)	1250	ecb_byteorder_helper (void)
1063	{	1251	{
1064	/* the union code still generates code under pressure in gcc, */	1252	/* the union code still generates code under pressure in gcc, */
1065	/* but less than using pointers, and always seems to */	1253	/* but less than using pointers, and always seems to */
1066	/* successfully return a constant. */	1254	/* successfully return a constant. */
1067	/* the reason why we have this horrible preprocessor mess */	1255	/* the reason why we have this horrible preprocessor mess */
1068	/* is to avoid it in all cases, at least on common architectures */	1256	/* is to avoid it in all cases, at least on common architectures */
1069	/* or when using a recent enough gcc version (>= 4.6) */	1257	/* or when using a recent enough gcc version (>= 4.6) */
1070	#if __i386 || __i386__ || _M_X86 || __amd64 || __amd64__ || _M_X64
1071	return 0x44;
1072	#elif __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_LITTLE_ENDIAN__	1258	#if (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_LITTLE_ENDIAN__) \
		1259	|| ((__i386 || __i386__ || _M_IX86 || ECB_GCC_AMD64 || ECB_MSVC_AMD64) && !__VOS__)
		1260	#define ECB_LITTLE_ENDIAN 1
1073	return 0x44;	1261	return 0x44332211;
1074	#elif __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__	1262	#elif (defined __BYTE_ORDER__ && __BYTE_ORDER__ == __ORDER_BIG_ENDIAN__) \
		1263	|| ((__AARCH64EB__ || __MIPSEB__ || __ARMEB__) && !__VOS__)
		1264	#define ECB_BIG_ENDIAN 1
1075	return 0x11;	1265	return 0x11223344;
1076	#else	1266	#else
1077	union	1267	union
1078	{	1268	{
		1269	uint8_t c[4];
1079	uint32_t i;	1270	uint32_t u;
1080	uint8_t c;
1081	} u = { 0x11223344 };	1271	} u = { 0x11, 0x22, 0x33, 0x44 };
1082	return u.c;	1272	return u.u;
1083	#endif	1273	#endif
1084	}	1274	}
1085		1275
1086	ecb_inline ecb_const ecb_bool ecb_big_endian (void);	1276	ecb_inline ecb_const ecb_bool ecb_big_endian (void);
1087	ecb_inline ecb_const ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11; }	1277	ecb_inline ecb_const ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11223344; }
1088	ecb_inline ecb_const ecb_bool ecb_little_endian (void);	1278	ecb_inline ecb_const ecb_bool ecb_little_endian (void);
1089	ecb_inline ecb_const ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44; }	1279	ecb_inline ecb_const ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44332211; }
1090		1280
1091	#if ECB_GCC_VERSION(3,0) || ECB_C99	1281	#if ECB_GCC_VERSION(3,0) || ECB_C99
1092	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))	1282	#define ecb_mod(m,n) ((m) % (n) + ((m) % (n) < 0 ? (n) : 0))
1093	#else	1283	#else
1094	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))	1284	#define ecb_mod(m,n) ((m) < 0 ? ((n) - 1 - ((-1 - (m)) % (n))) : ((m) % (n)))
…		…
1119	}	1309	}
1120	#else	1310	#else
1121	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))	1311	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))
1122	#endif	1312	#endif
1123		1313
		1314	ecb_function_ ecb_const uint32_t ecb_binary16_to_binary32 (uint32_t x);
		1315	ecb_function_ ecb_const uint32_t
		1316	ecb_binary16_to_binary32 (uint32_t x)
		1317	{
		1318	unsigned int s = (x & 0x8000) << (31 - 15);
		1319	int e = (x >> 10) & 0x001f;
		1320	unsigned int m = x & 0x03ff;
		1321
		1322	if (ecb_expect_false (e == 31))
		1323	/* infinity or NaN */
		1324	e = 255 - (127 - 15);
		1325	else if (ecb_expect_false (!e))
		1326	{
		1327	if (ecb_expect_true (!m))
		1328	/* zero, handled by code below by forcing e to 0 */
		1329	e = 0 - (127 - 15);
		1330	else
		1331	{
		1332	/* subnormal, renormalise */
		1333	unsigned int s = 10 - ecb_ld32 (m);
		1334
		1335	m = (m << s) & 0x3ff; /* mask implicit bit */
		1336	e -= s - 1;
		1337	}
		1338	}
		1339
		1340	/* e and m now are normalised, or zero, (or inf or nan) */
		1341	e += 127 - 15;
		1342
		1343	return s | (e << 23) | (m << (23 - 10));
		1344	}
		1345
		1346	ecb_function_ ecb_const uint16_t ecb_binary32_to_binary16 (uint32_t x);
		1347	ecb_function_ ecb_const uint16_t
		1348	ecb_binary32_to_binary16 (uint32_t x)
		1349	{
		1350	unsigned int s = (x >> 16) & 0x00008000; /* sign bit, the easy part */
		1351	unsigned int e = ((x >> 23) & 0x000000ff) - (127 - 15); /* the desired exponent */
		1352	unsigned int m = x & 0x007fffff;
		1353
		1354	x &= 0x7fffffff;
		1355
		1356	/* if it's within range of binary16 normals, use fast path */
		1357	if (ecb_expect_true (0x38800000 <= x && x <= 0x477fefff))
		1358	{
		1359	/* mantissa round-to-even */
		1360	m += 0x00000fff + ((m >> (23 - 10)) & 1);
		1361
		1362	/* handle overflow */
		1363	if (ecb_expect_false (m >= 0x00800000))
		1364	{
		1365	m >>= 1;
		1366	e += 1;
		1367	}
		1368
		1369	return s | (e << 10) | (m >> (23 - 10));
		1370	}
		1371
		1372	/* handle large numbers and infinity */
		1373	if (ecb_expect_true (0x477fefff < x && x <= 0x7f800000))
		1374	return s | 0x7c00;
		1375
		1376	/* handle zero, subnormals and small numbers */
		1377	if (ecb_expect_true (x < 0x38800000))
		1378	{
		1379	/* zero */
		1380	if (ecb_expect_true (!x))
		1381	return s;
		1382
		1383	/* handle subnormals */
		1384
		1385	/* too small, will be zero */
		1386	if (e < (14 - 24)) /* might not be sharp, but is good enough */
		1387	return s;
		1388
		1389	m |= 0x00800000; /* make implicit bit explicit */
		1390
		1391	/* very tricky - we need to round to the nearest e (+10) bit value */
		1392	{
		1393	unsigned int bits = 14 - e;
		1394	unsigned int half = (1 << (bits - 1)) - 1;
		1395	unsigned int even = (m >> bits) & 1;
		1396
		1397	/* if this overflows, we will end up with a normalised number */
		1398	m = (m + half + even) >> bits;
		1399	}
		1400
		1401	return s | m;
		1402	}
		1403
		1404	/* handle NaNs, preserve leftmost nan bits, but make sure we don't turn them into infinities */
		1405	m >>= 13;
		1406
		1407	return s | 0x7c00 | m | !m;
		1408	}
		1409
1124	/*******************************************************************************/	1410	/*******************************************************************************/
1125	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */	1411	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */
1126		1412
1127	/* basically, everything uses "ieee pure-endian" floating point numbers */	1413	/* basically, everything uses "ieee pure-endian" floating point numbers */
1128	/* the only noteworthy exception is ancient armle, which uses order 43218765 */	1414	/* the only noteworthy exception is ancient armle, which uses order 43218765 */
1129	#if 0 \	1415	#if 0 \
1130	|| __i386 || __i386__ \	1416	|| __i386 || __i386__ \
1131	|| __amd64 || __amd64__ || __x86_64 || __x86_64__ \	1417	|| ECB_GCC_AMD64 \
1132	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \	1418	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \
1133	|| defined __s390__ || defined __s390x__ \	1419	|| defined __s390__ || defined __s390x__ \
1134	|| defined __mips__ \	1420	|| defined __mips__ \
1135	|| defined __alpha__ \	1421	|| defined __alpha__ \
1136	|| defined __hppa__ \	1422	|| defined __hppa__ \
1137	|| defined __ia64__ \	1423	|| defined __ia64__ \
1138	|| defined __m68k__ \	1424	|| defined __m68k__ \
1139	|| defined __m88k__ \	1425	|| defined __m88k__ \
1140	|| defined __sh__ \	1426	|| defined __sh__ \
1141	|| defined _M_IX86 || defined _M_AMD64 || defined _M_IA64 \	1427	|| defined _M_IX86 || defined ECB_MSVC_AMD64 || defined _M_IA64 \
1142	|| (defined __arm__ && (defined __ARM_EABI__ || defined __EABI__ || defined __VFP_FP__ || defined _WIN32_WCE || defined __ANDROID__)) \	1428	|| (defined __arm__ && (defined __ARM_EABI__ || defined __EABI__ || defined __VFP_FP__ || defined _WIN32_WCE || defined __ANDROID__)) \
1143	|| defined __aarch64__	1429	|| defined __aarch64__
1144	#define ECB_STDFP 1	1430	#define ECB_STDFP 1
1145	#include <string.h> /* for memcpy */	1431	#include <string.h> /* for memcpy */
1146	#else	1432	#else
…		…
1164	#define ECB_NAN ECB_INFINITY	1450	#define ECB_NAN ECB_INFINITY
1165	#endif	1451	#endif
1166		1452
1167	#if ECB_C99 || _XOPEN_VERSION >= 600 || _POSIX_VERSION >= 200112L	1453	#if ECB_C99 || _XOPEN_VERSION >= 600 || _POSIX_VERSION >= 200112L
1168	#define ecb_ldexpf(x,e) ldexpf ((x), (e))	1454	#define ecb_ldexpf(x,e) ldexpf ((x), (e))
		1455	#define ecb_frexpf(x,e) frexpf ((x), (e))
1169	#else	1456	#else
1170	#define ecb_ldexpf(x,e) (float) ldexp ((x), (e))	1457	#define ecb_ldexpf(x,e) (float) ldexp ((double) (x), (e))
		1458	#define ecb_frexpf(x,e) (float) frexp ((double) (x), (e))
1171	#endif	1459	#endif
1172
1173	/* converts an ieee half/binary16 to a float */
1174	ecb_function_ ecb_const float ecb_binary16_to_float (uint16_t x);
1175	ecb_function_ ecb_const float
1176	ecb_binary16_to_float (uint16_t x)
1177	{
1178	int e = (x >> 10) & 0x1f;
1179	int m = x & 0x3ff;
1180	float r;
1181
1182	if (!e ) r = ecb_ldexpf (m , -24);
1183	else if (e != 31) r = ecb_ldexpf (m + 0x400, e - 25);
1184	else if (m ) r = ECB_NAN;
1185	else r = ECB_INFINITY;
1186
1187	return x & 0x8000 ? -r : r;
1188	}
1189		1460
1190	/* convert a float to ieee single/binary32 */	1461	/* convert a float to ieee single/binary32 */
1191	ecb_function_ ecb_const uint32_t ecb_float_to_binary32 (float x);	1462	ecb_function_ ecb_const uint32_t ecb_float_to_binary32 (float x);
1192	ecb_function_ ecb_const uint32_t	1463	ecb_function_ ecb_const uint32_t
1193	ecb_float_to_binary32 (float x)	1464	ecb_float_to_binary32 (float x)
…		…
1204	if (x == 0e0f ) return 0x00000000U;	1475	if (x == 0e0f ) return 0x00000000U;
1205	if (x > +3.40282346638528860e+38f) return 0x7f800000U;	1476	if (x > +3.40282346638528860e+38f) return 0x7f800000U;
1206	if (x < -3.40282346638528860e+38f) return 0xff800000U;	1477	if (x < -3.40282346638528860e+38f) return 0xff800000U;
1207	if (x != x ) return 0x7fbfffffU;	1478	if (x != x ) return 0x7fbfffffU;
1208		1479
1209	m = frexpf (x, &e) * 0x1000000U;	1480	m = ecb_frexpf (x, &e) * 0x1000000U;
1210		1481
1211	r = m & 0x80000000U;	1482	r = m & 0x80000000U;
1212		1483
1213	if (r)	1484	if (r)
1214	m = -m;	1485	m = -m;
…		…
1325	#endif	1596	#endif
1326		1597
1327	return r;	1598	return r;
1328	}	1599	}
1329		1600
		1601	/* convert a float to ieee half/binary16 */
		1602	ecb_function_ ecb_const uint16_t ecb_float_to_binary16 (float x);
		1603	ecb_function_ ecb_const uint16_t
		1604	ecb_float_to_binary16 (float x)
		1605	{
		1606	return ecb_binary32_to_binary16 (ecb_float_to_binary32 (x));
		1607	}
		1608
		1609	/* convert an ieee half/binary16 to float */
		1610	ecb_function_ ecb_const float ecb_binary16_to_float (uint16_t x);
		1611	ecb_function_ ecb_const float
		1612	ecb_binary16_to_float (uint16_t x)
		1613	{
		1614	return ecb_binary32_to_float (ecb_binary16_to_binary32 (x));
		1615	}
		1616
1330	#endif	1617	#endif
1331		1618
1332	#endif	1619	#endif
1333		1620
1334	/* ECB.H END */	1621	/* ECB.H END */
1335		1622
1336	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS	1623	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS
1337	/* if your architecture doesn't need memory fences, e.g. because it is	1624	/* if your architecture doesn't need memory fences, e.g. because it is
1338	* single-cpu/core, or if you use libev in a project that doesn't use libev	1625	* single-cpu/core, or if you use libev in a project that doesn't use libev
1339	* from multiple threads, then you can define ECB_AVOID_PTHREADS when compiling	1626	* from multiple threads, then you can define ECB_NO_THREADS when compiling
1340	* libev, in which cases the memory fences become nops.	1627	* libev, in which cases the memory fences become nops.
1341	* alternatively, you can remove this #error and link against libpthread,	1628	* alternatively, you can remove this #error and link against libpthread,
1342	* which will then provide the memory fences.	1629	* which will then provide the memory fences.
1343	*/	1630	*/
1344	# error "memory fences not defined for your architecture, please report"	1631	# error "memory fences not defined for your architecture, please report"
…		…
1348	# define ECB_MEMORY_FENCE do { } while (0)	1635	# define ECB_MEMORY_FENCE do { } while (0)
1349	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE	1636	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE
1350	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	1637	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
1351	#endif	1638	#endif
1352		1639
1353	#define expect_false(cond) ecb_expect_false (cond)
1354	#define expect_true(cond) ecb_expect_true (cond)
1355	#define noinline ecb_noinline
1356
1357	#define inline_size ecb_inline	1640	#define inline_size ecb_inline
1358		1641
1359	#if EV_FEATURE_CODE	1642	#if EV_FEATURE_CODE
1360	# define inline_speed ecb_inline	1643	# define inline_speed ecb_inline
1361	#else	1644	#else
1362	# define inline_speed static noinline	1645	# define inline_speed ecb_noinline static
1363	#endif	1646	#endif
		1647
		1648	/*****************************************************************************/
		1649	/* raw syscall wrappers */
		1650
		1651	#if EV_NEED_SYSCALL
		1652
		1653	#include <sys/syscall.h>
		1654
		1655	/*
		1656	* define some syscall wrappers for common architectures
		1657	* this is mostly for nice looks during debugging, not performance.
		1658	* our syscalls return < 0, not == -1, on error. which is good
		1659	* enough for linux aio.
		1660	* TODO: arm is also common nowadays, maybe even mips and x86
		1661	* TODO: after implementing this, it suddenly looks like overkill, but its hard to remove...
		1662	*/
		1663	#if __GNUC__ && __linux && ECB_AMD64 && !EV_FEATURE_CODE
		1664	/* the costly errno access probably kills this for size optimisation */
		1665
		1666	#define ev_syscall(nr,narg,arg1,arg2,arg3,arg4,arg5,arg6) \
		1667	({ \
		1668	long res; \
		1669	register unsigned long r6 __asm__ ("r9" ); \
		1670	register unsigned long r5 __asm__ ("r8" ); \
		1671	register unsigned long r4 __asm__ ("r10"); \
		1672	register unsigned long r3 __asm__ ("rdx"); \
		1673	register unsigned long r2 __asm__ ("rsi"); \
		1674	register unsigned long r1 __asm__ ("rdi"); \
		1675	if (narg >= 6) r6 = (unsigned long)(arg6); \
		1676	if (narg >= 5) r5 = (unsigned long)(arg5); \
		1677	if (narg >= 4) r4 = (unsigned long)(arg4); \
		1678	if (narg >= 3) r3 = (unsigned long)(arg3); \
		1679	if (narg >= 2) r2 = (unsigned long)(arg2); \
		1680	if (narg >= 1) r1 = (unsigned long)(arg1); \
		1681	__asm__ __volatile__ ( \
		1682	"syscall\n\t" \
		1683	: "=a" (res) \
		1684	: "0" (nr), "r" (r1), "r" (r2), "r" (r3), "r" (r4), "r" (r5) \
		1685	: "cc", "r11", "cx", "memory"); \
		1686	errno = -res; \
		1687	res; \
		1688	})
		1689
		1690	#endif
		1691
		1692	#ifdef ev_syscall
		1693	#define ev_syscall0(nr) ev_syscall (nr, 0, 0, 0, 0, 0, 0, 0)
		1694	#define ev_syscall1(nr,arg1) ev_syscall (nr, 1, arg1, 0, 0, 0, 0, 0)
		1695	#define ev_syscall2(nr,arg1,arg2) ev_syscall (nr, 2, arg1, arg2, 0, 0, 0, 0)
		1696	#define ev_syscall3(nr,arg1,arg2,arg3) ev_syscall (nr, 3, arg1, arg2, arg3, 0, 0, 0)
		1697	#define ev_syscall4(nr,arg1,arg2,arg3,arg4) ev_syscall (nr, 3, arg1, arg2, arg3, arg4, 0, 0)
		1698	#define ev_syscall5(nr,arg1,arg2,arg3,arg4,arg5) ev_syscall (nr, 5, arg1, arg2, arg3, arg4, arg5, 0)
		1699	#define ev_syscall6(nr,arg1,arg2,arg3,arg4,arg5,arg6) ev_syscall (nr, 6, arg1, arg2, arg3, arg4, arg5,arg6)
		1700	#else
		1701	#define ev_syscall0(nr) syscall (nr)
		1702	#define ev_syscall1(nr,arg1) syscall (nr, arg1)
		1703	#define ev_syscall2(nr,arg1,arg2) syscall (nr, arg1, arg2)
		1704	#define ev_syscall3(nr,arg1,arg2,arg3) syscall (nr, arg1, arg2, arg3)
		1705	#define ev_syscall4(nr,arg1,arg2,arg3,arg4) syscall (nr, arg1, arg2, arg3, arg4)
		1706	#define ev_syscall5(nr,arg1,arg2,arg3,arg4,arg5) syscall (nr, arg1, arg2, arg3, arg4, arg5)
		1707	#define ev_syscall6(nr,arg1,arg2,arg3,arg4,arg5,arg6) syscall (nr, arg1, arg2, arg3, arg4, arg5,arg6)
		1708	#endif
		1709
		1710	#endif
		1711
		1712	/*****************************************************************************/
1364		1713
1365	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)	1714	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)
1366		1715
1367	#if EV_MINPRI == EV_MAXPRI	1716	#if EV_MINPRI == EV_MAXPRI
1368	# define ABSPRI(w) (((W)w), 0)	1717	# define ABSPRI(w) (((W)w), 0)
1369	#else	1718	#else
1370	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)	1719	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)
1371	#endif	1720	#endif
1372		1721
1373	#define EMPTY /* required for microsofts broken pseudo-c compiler */	1722	#define EMPTY /* required for microsofts broken pseudo-c compiler */
1374	#define EMPTY2(a,b) /* used to suppress some warnings */
1375		1723
1376	typedef ev_watcher *W;	1724	typedef ev_watcher *W;
1377	typedef ev_watcher_list *WL;	1725	typedef ev_watcher_list *WL;
1378	typedef ev_watcher_time *WT;	1726	typedef ev_watcher_time *WT;
1379		1727
…		…
1404	# include "ev_win32.c"	1752	# include "ev_win32.c"
1405	#endif	1753	#endif
1406		1754
1407	/*****************************************************************************/	1755	/*****************************************************************************/
1408		1756
		1757	#if EV_USE_LINUXAIO
		1758	# include <linux/aio_abi.h> /* probably only needed for aio_context_t */
		1759	#endif
		1760
1409	/* define a suitable floor function (only used by periodics atm) */	1761	/* define a suitable floor function (only used by periodics atm) */
1410		1762
1411	#if EV_USE_FLOOR	1763	#if EV_USE_FLOOR
1412	# include <math.h>	1764	# include <math.h>
1413	# define ev_floor(v) floor (v)	1765	# define ev_floor(v) floor (v)
1414	#else	1766	#else
1415		1767
1416	#include <float.h>	1768	#include <float.h>
1417		1769
1418	/* a floor() replacement function, should be independent of ev_tstamp type */	1770	/* a floor() replacement function, should be independent of ev_tstamp type */
		1771	ecb_noinline
1419	static ev_tstamp noinline	1772	static ev_tstamp
1420	ev_floor (ev_tstamp v)	1773	ev_floor (ev_tstamp v)
1421	{	1774	{
1422	/* the choice of shift factor is not terribly important */	1775	/* the choice of shift factor is not terribly important */
1423	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */	1776	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */
1424	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;	1777	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;
1425	#else	1778	#else
1426	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;	1779	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;
1427	#endif	1780	#endif
1428		1781
		1782	/* special treatment for negative arguments */
		1783	if (ecb_expect_false (v < 0.))
		1784	{
		1785	ev_tstamp f = -ev_floor (-v);
		1786
		1787	return f - (f == v ? 0 : 1);
		1788	}
		1789
1429	/* argument too large for an unsigned long? */	1790	/* argument too large for an unsigned long? then reduce it */
1430	if (expect_false (v >= shift))	1791	if (ecb_expect_false (v >= shift))
1431	{	1792	{
1432	ev_tstamp f;	1793	ev_tstamp f;
1433		1794
1434	if (v == v - 1.)	1795	if (v == v - 1.)
1435	return v; /* very large number */	1796	return v; /* very large numbers are assumed to be integer */
1436		1797
1437	f = shift * ev_floor (v * (1. / shift));	1798	f = shift * ev_floor (v * (1. / shift));
1438	return f + ev_floor (v - f);	1799	return f + ev_floor (v - f);
1439	}	1800	}
1440		1801
1441	/* special treatment for negative args? */
1442	if (expect_false (v < 0.))
1443	{
1444	ev_tstamp f = -ev_floor (-v);
1445
1446	return f - (f == v ? 0 : 1);
1447	}
1448
1449	/* fits into an unsigned long */	1802	/* fits into an unsigned long */
1450	return (unsigned long)v;	1803	return (unsigned long)v;
1451	}	1804	}
1452		1805
1453	#endif	1806	#endif
…		…
1456		1809
1457	#ifdef __linux	1810	#ifdef __linux
1458	# include <sys/utsname.h>	1811	# include <sys/utsname.h>
1459	#endif	1812	#endif
1460		1813
1461	static unsigned int noinline ecb_cold	1814	ecb_noinline ecb_cold
		1815	static unsigned int
1462	ev_linux_version (void)	1816	ev_linux_version (void)
1463	{	1817	{
1464	#ifdef __linux	1818	#ifdef __linux
1465	unsigned int v = 0;	1819	unsigned int v = 0;
1466	struct utsname buf;	1820	struct utsname buf;
…		…
1495	}	1849	}
1496		1850
1497	/*****************************************************************************/	1851	/*****************************************************************************/
1498		1852
1499	#if EV_AVOID_STDIO	1853	#if EV_AVOID_STDIO
1500	static void noinline ecb_cold	1854	ecb_noinline ecb_cold
		1855	static void
1501	ev_printerr (const char *msg)	1856	ev_printerr (const char *msg)
1502	{	1857	{
1503	write (STDERR_FILENO, msg, strlen (msg));	1858	write (STDERR_FILENO, msg, strlen (msg));
1504	}	1859	}
1505	#endif	1860	#endif
1506		1861
1507	static void (*syserr_cb)(const char *msg) EV_THROW;	1862	static void (*syserr_cb)(const char *msg) EV_NOEXCEPT;
1508		1863
1509	void ecb_cold	1864	ecb_cold
		1865	void
1510	ev_set_syserr_cb (void (*cb)(const char *msg) EV_THROW) EV_THROW	1866	ev_set_syserr_cb (void (*cb)(const char *msg) EV_NOEXCEPT) EV_NOEXCEPT
1511	{	1867	{
1512	syserr_cb = cb;	1868	syserr_cb = cb;
1513	}	1869	}
1514		1870
1515	static void noinline ecb_cold	1871	ecb_noinline ecb_cold
		1872	static void
1516	ev_syserr (const char *msg)	1873	ev_syserr (const char *msg)
1517	{	1874	{
1518	if (!msg)	1875	if (!msg)
1519	msg = "(libev) system error";	1876	msg = "(libev) system error";
1520		1877
…		…
1533	abort ();	1890	abort ();
1534	}	1891	}
1535	}	1892	}
1536		1893
1537	static void *	1894	static void *
1538	ev_realloc_emul (void *ptr, long size) EV_THROW	1895	ev_realloc_emul (void *ptr, long size) EV_NOEXCEPT
1539	{	1896	{
1540	/* some systems, notably openbsd and darwin, fail to properly	1897	/* some systems, notably openbsd and darwin, fail to properly
1541	* implement realloc (x, 0) (as required by both ansi c-89 and	1898	* implement realloc (x, 0) (as required by both ansi c-89 and
1542	* the single unix specification, so work around them here.	1899	* the single unix specification, so work around them here.
1543	* recently, also (at least) fedora and debian started breaking it,	1900	* recently, also (at least) fedora and debian started breaking it,
…		…
1549		1906
1550	free (ptr);	1907	free (ptr);
1551	return 0;	1908	return 0;
1552	}	1909	}
1553		1910
1554	static void *(*alloc)(void *ptr, long size) EV_THROW = ev_realloc_emul;	1911	static void *(*alloc)(void *ptr, long size) EV_NOEXCEPT = ev_realloc_emul;
1555		1912
1556	void ecb_cold	1913	ecb_cold
		1914	void
1557	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_THROW) EV_THROW	1915	ev_set_allocator (void *(*cb)(void *ptr, long size) EV_NOEXCEPT) EV_NOEXCEPT
1558	{	1916	{
1559	alloc = cb;	1917	alloc = cb;
1560	}	1918	}
1561		1919
1562	inline_speed void *	1920	inline_speed void *
…		…
1589	typedef struct	1947	typedef struct
1590	{	1948	{
1591	WL head;	1949	WL head;
1592	unsigned char events; /* the events watched for */	1950	unsigned char events; /* the events watched for */
1593	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */	1951	unsigned char reify; /* flag set when this ANFD needs reification (EV_ANFD_REIFY, EV__IOFDSET) */
1594	unsigned char emask; /* the epoll backend stores the actual kernel mask in here */	1952	unsigned char emask; /* some backends store the actual kernel mask in here */
1595	unsigned char unused;	1953	unsigned char eflags; /* flags field for use by backends */
1596	#if EV_USE_EPOLL	1954	#if EV_USE_EPOLL
1597	unsigned int egen; /* generation counter to counter epoll bugs */	1955	unsigned int egen; /* generation counter to counter epoll bugs */
1598	#endif	1956	#endif
1599	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP	1957	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP
1600	SOCKET handle;	1958	SOCKET handle;
…		…
1654	static struct ev_loop default_loop_struct;	2012	static struct ev_loop default_loop_struct;
1655	EV_API_DECL struct ev_loop *ev_default_loop_ptr = 0; /* needs to be initialised to make it a definition despite extern */	2013	EV_API_DECL struct ev_loop *ev_default_loop_ptr = 0; /* needs to be initialised to make it a definition despite extern */
1656		2014
1657	#else	2015	#else
1658		2016
1659	EV_API_DECL ev_tstamp ev_rt_now = 0; /* needs to be initialised to make it a definition despite extern */	2017	EV_API_DECL ev_tstamp ev_rt_now = EV_TS_CONST (0.); /* needs to be initialised to make it a definition despite extern */
1660	#define VAR(name,decl) static decl;	2018	#define VAR(name,decl) static decl;
1661	#include "ev_vars.h"	2019	#include "ev_vars.h"
1662	#undef VAR	2020	#undef VAR
1663		2021
1664	static int ev_default_loop_ptr;	2022	static int ev_default_loop_ptr;
1665		2023
1666	#endif	2024	#endif
1667		2025
1668	#if EV_FEATURE_API	2026	#if EV_FEATURE_API
1669	# define EV_RELEASE_CB if (expect_false (release_cb)) release_cb (EV_A)	2027	# define EV_RELEASE_CB if (ecb_expect_false (release_cb)) release_cb (EV_A)
1670	# define EV_ACQUIRE_CB if (expect_false (acquire_cb)) acquire_cb (EV_A)	2028	# define EV_ACQUIRE_CB if (ecb_expect_false (acquire_cb)) acquire_cb (EV_A)
1671	# define EV_INVOKE_PENDING invoke_cb (EV_A)	2029	# define EV_INVOKE_PENDING invoke_cb (EV_A)
1672	#else	2030	#else
1673	# define EV_RELEASE_CB (void)0	2031	# define EV_RELEASE_CB (void)0
1674	# define EV_ACQUIRE_CB (void)0	2032	# define EV_ACQUIRE_CB (void)0
1675	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)	2033	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)
…		…
1679		2037
1680	/*****************************************************************************/	2038	/*****************************************************************************/
1681		2039
1682	#ifndef EV_HAVE_EV_TIME	2040	#ifndef EV_HAVE_EV_TIME
1683	ev_tstamp	2041	ev_tstamp
1684	ev_time (void) EV_THROW	2042	ev_time (void) EV_NOEXCEPT
1685	{	2043	{
1686	#if EV_USE_REALTIME	2044	#if EV_USE_REALTIME
1687	if (expect_true (have_realtime))	2045	if (ecb_expect_true (have_realtime))
1688	{	2046	{
1689	struct timespec ts;	2047	struct timespec ts;
1690	clock_gettime (CLOCK_REALTIME, &ts);	2048	clock_gettime (CLOCK_REALTIME, &ts);
1691	return ts.tv_sec + ts.tv_nsec * 1e-9;	2049	return EV_TS_GET (ts);
1692	}	2050	}
1693	#endif	2051	#endif
1694		2052
		2053	{
1695	struct timeval tv;	2054	struct timeval tv;
1696	gettimeofday (&tv, 0);	2055	gettimeofday (&tv, 0);
1697	return tv.tv_sec + tv.tv_usec * 1e-6;	2056	return EV_TV_GET (tv);
		2057	}
1698	}	2058	}
1699	#endif	2059	#endif
1700		2060
1701	inline_size ev_tstamp	2061	inline_size ev_tstamp
1702	get_clock (void)	2062	get_clock (void)
1703	{	2063	{
1704	#if EV_USE_MONOTONIC	2064	#if EV_USE_MONOTONIC
1705	if (expect_true (have_monotonic))	2065	if (ecb_expect_true (have_monotonic))
1706	{	2066	{
1707	struct timespec ts;	2067	struct timespec ts;
1708	clock_gettime (CLOCK_MONOTONIC, &ts);	2068	clock_gettime (CLOCK_MONOTONIC, &ts);
1709	return ts.tv_sec + ts.tv_nsec * 1e-9;	2069	return EV_TS_GET (ts);
1710	}	2070	}
1711	#endif	2071	#endif
1712		2072
1713	return ev_time ();	2073	return ev_time ();
1714	}	2074	}
1715		2075
1716	#if EV_MULTIPLICITY	2076	#if EV_MULTIPLICITY
1717	ev_tstamp	2077	ev_tstamp
1718	ev_now (EV_P) EV_THROW	2078	ev_now (EV_P) EV_NOEXCEPT
1719	{	2079	{
1720	return ev_rt_now;	2080	return ev_rt_now;
1721	}	2081	}
1722	#endif	2082	#endif
1723		2083
1724	void	2084	void
1725	ev_sleep (ev_tstamp delay) EV_THROW	2085	ev_sleep (ev_tstamp delay) EV_NOEXCEPT
1726	{	2086	{
1727	if (delay > 0.)	2087	if (delay > EV_TS_CONST (0.))
1728	{	2088	{
1729	#if EV_USE_NANOSLEEP	2089	#if EV_USE_NANOSLEEP
1730	struct timespec ts;	2090	struct timespec ts;
1731		2091
1732	EV_TS_SET (ts, delay);	2092	EV_TS_SET (ts, delay);
1733	nanosleep (&ts, 0);	2093	nanosleep (&ts, 0);
1734	#elif defined _WIN32	2094	#elif defined _WIN32
		2095	/* maybe this should round up, as ms is very low resolution */
		2096	/* compared to select (µs) or nanosleep (ns) */
1735	Sleep ((unsigned long)(delay * 1e3));	2097	Sleep ((unsigned long)(EV_TS_TO_MSEC (delay)));
1736	#else	2098	#else
1737	struct timeval tv;	2099	struct timeval tv;
1738		2100
1739	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */	2101	/* here we rely on sys/time.h + sys/types.h + unistd.h providing select */
1740	/* something not guaranteed by newer posix versions, but guaranteed */	2102	/* something not guaranteed by newer posix versions, but guaranteed */
…		…
1770	}	2132	}
1771		2133
1772	return ncur;	2134	return ncur;
1773	}	2135	}
1774		2136
1775	static void * noinline ecb_cold	2137	ecb_noinline ecb_cold
		2138	static void *
1776	array_realloc (int elem, void *base, int *cur, int cnt)	2139	array_realloc (int elem, void *base, int *cur, int cnt)
1777	{	2140	{
1778	*cur = array_nextsize (elem, *cur, cnt);	2141	*cur = array_nextsize (elem, *cur, cnt);
1779	return ev_realloc (base, elem * *cur);	2142	return ev_realloc (base, elem * *cur);
1780	}	2143	}
1781		2144
		2145	#define array_needsize_noinit(base,offset,count)
		2146
1782	#define array_init_zero(base,count) \	2147	#define array_needsize_zerofill(base,offset,count) \
1783	memset ((void *)(base), 0, sizeof (*(base)) * (count))	2148	memset ((void *)(base + offset), 0, sizeof (*(base)) * (count))
1784		2149
1785	#define array_needsize(type,base,cur,cnt,init) \	2150	#define array_needsize(type,base,cur,cnt,init) \
1786	if (expect_false ((cnt) > (cur))) \	2151	if (ecb_expect_false ((cnt) > (cur))) \
1787	{ \	2152	{ \
1788	int ecb_unused ocur_ = (cur); \	2153	ecb_unused int ocur_ = (cur); \
1789	(base) = (type *)array_realloc \	2154	(base) = (type *)array_realloc \
1790	(sizeof (type), (base), &(cur), (cnt)); \	2155	(sizeof (type), (base), &(cur), (cnt)); \
1791	init ((base) + (ocur_), (cur) - ocur_); \	2156	init ((base), ocur_, ((cur) - ocur_)); \
1792	}	2157	}
1793		2158
1794	#if 0	2159	#if 0
1795	#define array_slim(type,stem) \	2160	#define array_slim(type,stem) \
1796	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \	2161	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \
…		…
1805	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0	2170	ev_free (stem ## s idx); stem ## cnt idx = stem ## max idx = 0; stem ## s idx = 0
1806		2171
1807	/*****************************************************************************/	2172	/*****************************************************************************/
1808		2173
1809	/* dummy callback for pending events */	2174	/* dummy callback for pending events */
1810	static void noinline	2175	ecb_noinline
		2176	static void
1811	pendingcb (EV_P_ ev_prepare *w, int revents)	2177	pendingcb (EV_P_ ev_prepare *w, int revents)
1812	{	2178	{
1813	}	2179	}
1814		2180
1815	void noinline	2181	ecb_noinline
		2182	void
1816	ev_feed_event (EV_P_ void *w, int revents) EV_THROW	2183	ev_feed_event (EV_P_ void *w, int revents) EV_NOEXCEPT
1817	{	2184	{
1818	W w_ = (W)w;	2185	W w_ = (W)w;
1819	int pri = ABSPRI (w_);	2186	int pri = ABSPRI (w_);
1820		2187
1821	if (expect_false (w_->pending))	2188	if (ecb_expect_false (w_->pending))
1822	pendings [pri][w_->pending - 1].events |= revents;	2189	pendings [pri][w_->pending - 1].events |= revents;
1823	else	2190	else
1824	{	2191	{
1825	w_->pending = ++pendingcnt [pri];	2192	w_->pending = ++pendingcnt [pri];
1826	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, EMPTY2);	2193	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, array_needsize_noinit);
1827	pendings [pri][w_->pending - 1].w = w_;	2194	pendings [pri][w_->pending - 1].w = w_;
1828	pendings [pri][w_->pending - 1].events = revents;	2195	pendings [pri][w_->pending - 1].events = revents;
1829	}	2196	}
1830		2197
1831	pendingpri = NUMPRI - 1;	2198	pendingpri = NUMPRI - 1;
1832	}	2199	}
1833		2200
1834	inline_speed void	2201	inline_speed void
1835	feed_reverse (EV_P_ W w)	2202	feed_reverse (EV_P_ W w)
1836	{	2203	{
1837	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, EMPTY2);	2204	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, array_needsize_noinit);
1838	rfeeds [rfeedcnt++] = w;	2205	rfeeds [rfeedcnt++] = w;
1839	}	2206	}
1840		2207
1841	inline_size void	2208	inline_size void
1842	feed_reverse_done (EV_P_ int revents)	2209	feed_reverse_done (EV_P_ int revents)
…		…
1877	inline_speed void	2244	inline_speed void
1878	fd_event (EV_P_ int fd, int revents)	2245	fd_event (EV_P_ int fd, int revents)
1879	{	2246	{
1880	ANFD *anfd = anfds + fd;	2247	ANFD *anfd = anfds + fd;
1881		2248
1882	if (expect_true (!anfd->reify))	2249	if (ecb_expect_true (!anfd->reify))
1883	fd_event_nocheck (EV_A_ fd, revents);	2250	fd_event_nocheck (EV_A_ fd, revents);
1884	}	2251	}
1885		2252
1886	void	2253	void
1887	ev_feed_fd_event (EV_P_ int fd, int revents) EV_THROW	2254	ev_feed_fd_event (EV_P_ int fd, int revents) EV_NOEXCEPT
1888	{	2255	{
1889	if (fd >= 0 && fd < anfdmax)	2256	if (fd >= 0 && fd < anfdmax)
1890	fd_event_nocheck (EV_A_ fd, revents);	2257	fd_event_nocheck (EV_A_ fd, revents);
1891	}	2258	}
1892		2259
…		…
1895	inline_size void	2262	inline_size void
1896	fd_reify (EV_P)	2263	fd_reify (EV_P)
1897	{	2264	{
1898	int i;	2265	int i;
1899		2266
		2267	/* most backends do not modify the fdchanges list in backend_modfiy.
		2268	* except io_uring, which has fixed-size buffers which might force us
		2269	* to handle events in backend_modify, causing fdchangesd to be amended,
		2270	* which could result in an endless loop.
		2271	* to avoid this, we do not dynamically handle fds that were added
		2272	* during fd_reify. that menas thast for those backends, fdchangecnt
		2273	* might be non-zero during poll, which must cause them to not block.
		2274	* to not put too much of a burden on other backends, this detail
		2275	* needs to be handled in the backend.
		2276	*/
		2277	int changecnt = fdchangecnt;
		2278
1900	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP	2279	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP
1901	for (i = 0; i < fdchangecnt; ++i)	2280	for (i = 0; i < changecnt; ++i)
1902	{	2281	{
1903	int fd = fdchanges [i];	2282	int fd = fdchanges [i];
1904	ANFD *anfd = anfds + fd;	2283	ANFD *anfd = anfds + fd;
1905		2284
1906	if (anfd->reify & EV__IOFDSET && anfd->head)	2285	if (anfd->reify & EV__IOFDSET && anfd->head)
…		…
1920	}	2299	}
1921	}	2300	}
1922	}	2301	}
1923	#endif	2302	#endif
1924		2303
1925	for (i = 0; i < fdchangecnt; ++i)	2304	for (i = 0; i < changecnt; ++i)
1926	{	2305	{
1927	int fd = fdchanges [i];	2306	int fd = fdchanges [i];
1928	ANFD *anfd = anfds + fd;	2307	ANFD *anfd = anfds + fd;
1929	ev_io *w;	2308	ev_io *w;
1930		2309
1931	unsigned char o_events = anfd->events;	2310	unsigned char o_events = anfd->events;
1932	unsigned char o_reify = anfd->reify;	2311	unsigned char o_reify = anfd->reify;
1933		2312
1934	anfd->reify = 0;	2313	anfd->reify = 0;
1935		2314
1936	/*if (expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */	2315	/*if (ecb_expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */
1937	{	2316	{
1938	anfd->events = 0;	2317	anfd->events = 0;
1939		2318
1940	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)	2319	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)
1941	anfd->events |= (unsigned char)w->events;	2320	anfd->events |= (unsigned char)w->events;
…		…
1946		2325
1947	if (o_reify & EV__IOFDSET)	2326	if (o_reify & EV__IOFDSET)
1948	backend_modify (EV_A_ fd, o_events, anfd->events);	2327	backend_modify (EV_A_ fd, o_events, anfd->events);
1949	}	2328	}
1950		2329
		2330	/* normally, fdchangecnt hasn't changed. if it has, then new fds have been added.
		2331	* this is a rare case (see beginning comment in this function), so we copy them to the
		2332	* front and hope the backend handles this case.
		2333	*/
		2334	if (ecb_expect_false (fdchangecnt != changecnt))
		2335	memmove (fdchanges, fdchanges + changecnt, (fdchangecnt - changecnt) * sizeof (*fdchanges));
		2336
1951	fdchangecnt = 0;	2337	fdchangecnt -= changecnt;
1952	}	2338	}
1953		2339
1954	/* something about the given fd changed */	2340	/* something about the given fd changed */
1955	inline_size void	2341	inline_size
		2342	void
1956	fd_change (EV_P_ int fd, int flags)	2343	fd_change (EV_P_ int fd, int flags)
1957	{	2344	{
1958	unsigned char reify = anfds [fd].reify;	2345	unsigned char reify = anfds [fd].reify;
1959	anfds [fd].reify |= flags;	2346	anfds [fd].reify |= flags;
1960		2347
1961	if (expect_true (!reify))	2348	if (ecb_expect_true (!reify))
1962	{	2349	{
1963	++fdchangecnt;	2350	++fdchangecnt;
1964	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, EMPTY2);	2351	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, array_needsize_noinit);
1965	fdchanges [fdchangecnt - 1] = fd;	2352	fdchanges [fdchangecnt - 1] = fd;
1966	}	2353	}
1967	}	2354	}
1968		2355
1969	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */	2356	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */
1970	inline_speed void ecb_cold	2357	inline_speed ecb_cold void
1971	fd_kill (EV_P_ int fd)	2358	fd_kill (EV_P_ int fd)
1972	{	2359	{
1973	ev_io *w;	2360	ev_io *w;
1974		2361
1975	while ((w = (ev_io *)anfds [fd].head))	2362	while ((w = (ev_io *)anfds [fd].head))
…		…
1978	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);	2365	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);
1979	}	2366	}
1980	}	2367	}
1981		2368
1982	/* check whether the given fd is actually valid, for error recovery */	2369	/* check whether the given fd is actually valid, for error recovery */
1983	inline_size int ecb_cold	2370	inline_size ecb_cold int
1984	fd_valid (int fd)	2371	fd_valid (int fd)
1985	{	2372	{
1986	#ifdef _WIN32	2373	#ifdef _WIN32
1987	return EV_FD_TO_WIN32_HANDLE (fd) != -1;	2374	return EV_FD_TO_WIN32_HANDLE (fd) != -1;
1988	#else	2375	#else
1989	return fcntl (fd, F_GETFD) != -1;	2376	return fcntl (fd, F_GETFD) != -1;
1990	#endif	2377	#endif
1991	}	2378	}
1992		2379
1993	/* called on EBADF to verify fds */	2380	/* called on EBADF to verify fds */
1994	static void noinline ecb_cold	2381	ecb_noinline ecb_cold
		2382	static void
1995	fd_ebadf (EV_P)	2383	fd_ebadf (EV_P)
1996	{	2384	{
1997	int fd;	2385	int fd;
1998		2386
1999	for (fd = 0; fd < anfdmax; ++fd)	2387	for (fd = 0; fd < anfdmax; ++fd)
…		…
2001	if (!fd_valid (fd) && errno == EBADF)	2389	if (!fd_valid (fd) && errno == EBADF)
2002	fd_kill (EV_A_ fd);	2390	fd_kill (EV_A_ fd);
2003	}	2391	}
2004		2392
2005	/* called on ENOMEM in select/poll to kill some fds and retry */	2393	/* called on ENOMEM in select/poll to kill some fds and retry */
2006	static void noinline ecb_cold	2394	ecb_noinline ecb_cold
		2395	static void
2007	fd_enomem (EV_P)	2396	fd_enomem (EV_P)
2008	{	2397	{
2009	int fd;	2398	int fd;
2010		2399
2011	for (fd = anfdmax; fd--; )	2400	for (fd = anfdmax; fd--; )
…		…
2015	break;	2404	break;
2016	}	2405	}
2017	}	2406	}
2018		2407
2019	/* usually called after fork if backend needs to re-arm all fds from scratch */	2408	/* usually called after fork if backend needs to re-arm all fds from scratch */
2020	static void noinline	2409	ecb_noinline
		2410	static void
2021	fd_rearm_all (EV_P)	2411	fd_rearm_all (EV_P)
2022	{	2412	{
2023	int fd;	2413	int fd;
2024		2414
2025	for (fd = 0; fd < anfdmax; ++fd)	2415	for (fd = 0; fd < anfdmax; ++fd)
…		…
2078	ev_tstamp minat;	2468	ev_tstamp minat;
2079	ANHE *minpos;	2469	ANHE *minpos;
2080	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;	2470	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;
2081		2471
2082	/* find minimum child */	2472	/* find minimum child */
2083	if (expect_true (pos + DHEAP - 1 < E))	2473	if (ecb_expect_true (pos + DHEAP - 1 < E))
2084	{	2474	{
2085	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));	2475	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));
2086	if ( ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));	2476	if ( minat > ANHE_at (pos [1])) (minpos = pos + 1), (minat = ANHE_at (*minpos));
2087	if ( ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));	2477	if ( minat > ANHE_at (pos [2])) (minpos = pos + 2), (minat = ANHE_at (*minpos));
2088	if ( ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));	2478	if ( minat > ANHE_at (pos [3])) (minpos = pos + 3), (minat = ANHE_at (*minpos));
2089	}	2479	}
2090	else if (pos < E)	2480	else if (pos < E)
2091	{	2481	{
2092	/* slow path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));	2482	/* slow path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));
2093	if (pos + 1 < E && ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));	2483	if (pos + 1 < E && minat > ANHE_at (pos [1])) (minpos = pos + 1), (minat = ANHE_at (*minpos));
2094	if (pos + 2 < E && ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));	2484	if (pos + 2 < E && minat > ANHE_at (pos [2])) (minpos = pos + 2), (minat = ANHE_at (*minpos));
2095	if (pos + 3 < E && ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));	2485	if (pos + 3 < E && minat > ANHE_at (pos [3])) (minpos = pos + 3), (minat = ANHE_at (*minpos));
2096	}	2486	}
2097	else	2487	else
2098	break;	2488	break;
2099		2489
2100	if (ANHE_at (he) <= minat)	2490	if (ANHE_at (he) <= minat)
…		…
2108		2498
2109	heap [k] = he;	2499	heap [k] = he;
2110	ev_active (ANHE_w (he)) = k;	2500	ev_active (ANHE_w (he)) = k;
2111	}	2501	}
2112		2502
2113	#else /* 4HEAP */	2503	#else /* not 4HEAP */
2114		2504
2115	#define HEAP0 1	2505	#define HEAP0 1
2116	#define HPARENT(k) ((k) >> 1)	2506	#define HPARENT(k) ((k) >> 1)
2117	#define UPHEAP_DONE(p,k) (!(p))	2507	#define UPHEAP_DONE(p,k) (!(p))
2118		2508
…		…
2206		2596
2207	/*****************************************************************************/	2597	/*****************************************************************************/
2208		2598
2209	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	2599	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2210		2600
2211	static void noinline ecb_cold	2601	ecb_noinline ecb_cold
		2602	static void
2212	evpipe_init (EV_P)	2603	evpipe_init (EV_P)
2213	{	2604	{
2214	if (!ev_is_active (&pipe_w))	2605	if (!ev_is_active (&pipe_w))
2215	{	2606	{
2216	int fds [2];	2607	int fds [2];
…		…
2256	inline_speed void	2647	inline_speed void
2257	evpipe_write (EV_P_ EV_ATOMIC_T *flag)	2648	evpipe_write (EV_P_ EV_ATOMIC_T *flag)
2258	{	2649	{
2259	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */	2650	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */
2260		2651
2261	if (expect_true (*flag))	2652	if (ecb_expect_true (*flag))
2262	return;	2653	return;
2263		2654
2264	*flag = 1;	2655	*flag = 1;
2265	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */	2656	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */
2266		2657
…		…
2287	#endif	2678	#endif
2288	{	2679	{
2289	#ifdef _WIN32	2680	#ifdef _WIN32
2290	WSABUF buf;	2681	WSABUF buf;
2291	DWORD sent;	2682	DWORD sent;
2292	buf.buf = &buf;	2683	buf.buf = (char *)&buf;
2293	buf.len = 1;	2684	buf.len = 1;
2294	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);	2685	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);
2295	#else	2686	#else
2296	write (evpipe [1], &(evpipe [1]), 1);	2687	write (evpipe [1], &(evpipe [1]), 1);
2297	#endif	2688	#endif
…		…
2343	sig_pending = 0;	2734	sig_pending = 0;
2344		2735
2345	ECB_MEMORY_FENCE;	2736	ECB_MEMORY_FENCE;
2346		2737
2347	for (i = EV_NSIG - 1; i--; )	2738	for (i = EV_NSIG - 1; i--; )
2348	if (expect_false (signals [i].pending))	2739	if (ecb_expect_false (signals [i].pending))
2349	ev_feed_signal_event (EV_A_ i + 1);	2740	ev_feed_signal_event (EV_A_ i + 1);
2350	}	2741	}
2351	#endif	2742	#endif
2352		2743
2353	#if EV_ASYNC_ENABLE	2744	#if EV_ASYNC_ENABLE
…		…
2369	}	2760	}
2370		2761
2371	/*****************************************************************************/	2762	/*****************************************************************************/
2372		2763
2373	void	2764	void
2374	ev_feed_signal (int signum) EV_THROW	2765	ev_feed_signal (int signum) EV_NOEXCEPT
2375	{	2766	{
2376	#if EV_MULTIPLICITY	2767	#if EV_MULTIPLICITY
2377	EV_P;	2768	EV_P;
2378	ECB_MEMORY_FENCE_ACQUIRE;	2769	ECB_MEMORY_FENCE_ACQUIRE;
2379	EV_A = signals [signum - 1].loop;	2770	EV_A = signals [signum - 1].loop;
…		…
2394	#endif	2785	#endif
2395		2786
2396	ev_feed_signal (signum);	2787	ev_feed_signal (signum);
2397	}	2788	}
2398		2789
2399	void noinline	2790	ecb_noinline
		2791	void
2400	ev_feed_signal_event (EV_P_ int signum) EV_THROW	2792	ev_feed_signal_event (EV_P_ int signum) EV_NOEXCEPT
2401	{	2793	{
2402	WL w;	2794	WL w;
2403		2795
2404	if (expect_false (signum <= 0 || signum >= EV_NSIG))	2796	if (ecb_expect_false (signum <= 0 || signum >= EV_NSIG))
2405	return;	2797	return;
2406		2798
2407	--signum;	2799	--signum;
2408		2800
2409	#if EV_MULTIPLICITY	2801	#if EV_MULTIPLICITY
2410	/* it is permissible to try to feed a signal to the wrong loop */	2802	/* it is permissible to try to feed a signal to the wrong loop */
2411	/* or, likely more useful, feeding a signal nobody is waiting for */	2803	/* or, likely more useful, feeding a signal nobody is waiting for */
2412		2804
2413	if (expect_false (signals [signum].loop != EV_A))	2805	if (ecb_expect_false (signals [signum].loop != EV_A))
2414	return;	2806	return;
2415	#endif	2807	#endif
2416		2808
2417	signals [signum].pending = 0;	2809	signals [signum].pending = 0;
2418	ECB_MEMORY_FENCE_RELEASE;	2810	ECB_MEMORY_FENCE_RELEASE;
…		…
2502		2894
2503	#endif	2895	#endif
2504		2896
2505	/*****************************************************************************/	2897	/*****************************************************************************/
2506		2898
		2899	#if EV_USE_TIMERFD
		2900
		2901	static void periodics_reschedule (EV_P);
		2902
		2903	static void
		2904	timerfdcb (EV_P_ ev_io *iow, int revents)
		2905	{
		2906	struct itimerspec its = { 0 };
		2907
		2908	/* since we can't easily come zup with a (portable) maximum value of time_t,
		2909	* we wake up once per month, which hopefully is rare enough to not
		2910	* be a problem. */
		2911	its.it_value.tv_sec = ev_rt_now + 86400 * 30;
		2912	timerfd_settime (timerfd, TFD_TIMER_ABSTIME | TFD_TIMER_CANCEL_ON_SET, &its, 0);
		2913
		2914	ev_rt_now = ev_time ();
		2915	/* periodics_reschedule only needs ev_rt_now */
		2916	/* but maybe in the future we want the full treatment. */
		2917	/*
		2918	now_floor = EV_TS_CONST (0.);
		2919	time_update (EV_A_ EV_TSTAMP_HUGE);
		2920	*/
		2921	periodics_reschedule (EV_A);
		2922	}
		2923
		2924	ecb_noinline ecb_cold
		2925	static void
		2926	evtimerfd_init (EV_P)
		2927	{
		2928	if (!ev_is_active (&timerfd_w))
		2929	{
		2930	timerfd = timerfd_create (CLOCK_REALTIME, TFD_NONBLOCK | TFD_CLOEXEC);
		2931
		2932	if (timerfd >= 0)
		2933	{
		2934	fd_intern (timerfd); /* just to be sure */
		2935
		2936	ev_io_init (&timerfd_w, timerfdcb, timerfd, EV_READ);
		2937	ev_set_priority (&timerfd_w, EV_MINPRI);
		2938	ev_io_start (EV_A_ &timerfd_w);
		2939	ev_unref (EV_A); /* watcher should not keep loop alive */
		2940
		2941	/* (re-) arm timer */
		2942	timerfdcb (EV_A_ 0, 0);
		2943	}
		2944	}
		2945	}
		2946
		2947	#endif
		2948
		2949	/*****************************************************************************/
		2950
2507	#if EV_USE_IOCP	2951	#if EV_USE_IOCP
2508	# include "ev_iocp.c"	2952	# include "ev_iocp.c"
2509	#endif	2953	#endif
2510	#if EV_USE_PORT	2954	#if EV_USE_PORT
2511	# include "ev_port.c"	2955	# include "ev_port.c"
…		…
2514	# include "ev_kqueue.c"	2958	# include "ev_kqueue.c"
2515	#endif	2959	#endif
2516	#if EV_USE_EPOLL	2960	#if EV_USE_EPOLL
2517	# include "ev_epoll.c"	2961	# include "ev_epoll.c"
2518	#endif	2962	#endif
		2963	#if EV_USE_LINUXAIO
		2964	# include "ev_linuxaio.c"
		2965	#endif
		2966	#if EV_USE_IOURING
		2967	# include "ev_iouring.c"
		2968	#endif
2519	#if EV_USE_POLL	2969	#if EV_USE_POLL
2520	# include "ev_poll.c"	2970	# include "ev_poll.c"
2521	#endif	2971	#endif
2522	#if EV_USE_SELECT	2972	#if EV_USE_SELECT
2523	# include "ev_select.c"	2973	# include "ev_select.c"
2524	#endif	2974	#endif
2525		2975
2526	int ecb_cold	2976	ecb_cold int
2527	ev_version_major (void) EV_THROW	2977	ev_version_major (void) EV_NOEXCEPT
2528	{	2978	{
2529	return EV_VERSION_MAJOR;	2979	return EV_VERSION_MAJOR;
2530	}	2980	}
2531		2981
2532	int ecb_cold	2982	ecb_cold int
2533	ev_version_minor (void) EV_THROW	2983	ev_version_minor (void) EV_NOEXCEPT
2534	{	2984	{
2535	return EV_VERSION_MINOR;	2985	return EV_VERSION_MINOR;
2536	}	2986	}
2537		2987
2538	/* return true if we are running with elevated privileges and should ignore env variables */	2988	/* return true if we are running with elevated privileges and should ignore env variables */
2539	int inline_size ecb_cold	2989	inline_size ecb_cold int
2540	enable_secure (void)	2990	enable_secure (void)
2541	{	2991	{
2542	#ifdef _WIN32	2992	#ifdef _WIN32
2543	return 0;	2993	return 0;
2544	#else	2994	#else
2545	return getuid () != geteuid ()	2995	return getuid () != geteuid ()
2546	|| getgid () != getegid ();	2996	|| getgid () != getegid ();
2547	#endif	2997	#endif
2548	}	2998	}
2549		2999
2550	unsigned int ecb_cold	3000	ecb_cold
		3001	unsigned int
2551	ev_supported_backends (void) EV_THROW	3002	ev_supported_backends (void) EV_NOEXCEPT
2552	{	3003	{
2553	unsigned int flags = 0;	3004	unsigned int flags = 0;
2554		3005
2555	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;	3006	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;
2556	if (EV_USE_KQUEUE) flags |= EVBACKEND_KQUEUE;	3007	if (EV_USE_KQUEUE ) flags |= EVBACKEND_KQUEUE;
2557	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;	3008	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;
2558	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;	3009	if (EV_USE_LINUXAIO ) flags |= EVBACKEND_LINUXAIO;
2559	if (EV_USE_SELECT) flags |= EVBACKEND_SELECT;	3010	if (EV_USE_IOURING && ev_linux_version () >= 0x050601) flags |= EVBACKEND_IOURING; /* 5.6.1+ */
2560		3011	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;
		3012	if (EV_USE_SELECT ) flags |= EVBACKEND_SELECT;
		3013
2561	return flags;	3014	return flags;
2562	}	3015	}
2563		3016
2564	unsigned int ecb_cold	3017	ecb_cold
		3018	unsigned int
2565	ev_recommended_backends (void) EV_THROW	3019	ev_recommended_backends (void) EV_NOEXCEPT
2566	{	3020	{
2567	unsigned int flags = ev_supported_backends ();	3021	unsigned int flags = ev_supported_backends ();
2568		3022
2569	#ifndef __NetBSD__	3023	#ifndef __NetBSD__
2570	/* kqueue is borked on everything but netbsd apparently */	3024	/* kqueue is borked on everything but netbsd apparently */
…		…
2578	#endif	3032	#endif
2579	#ifdef __FreeBSD__	3033	#ifdef __FreeBSD__
2580	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */	3034	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */
2581	#endif	3035	#endif
2582		3036
		3037	/* TODO: linuxaio is very experimental */
		3038	#if !EV_RECOMMEND_LINUXAIO
		3039	flags &= ~EVBACKEND_LINUXAIO;
		3040	#endif
		3041	/* TODO: linuxaio is super experimental */
		3042	#if !EV_RECOMMEND_IOURING
		3043	flags &= ~EVBACKEND_IOURING;
		3044	#endif
		3045
2583	return flags;	3046	return flags;
2584	}	3047	}
2585		3048
2586	unsigned int ecb_cold	3049	ecb_cold
		3050	unsigned int
2587	ev_embeddable_backends (void) EV_THROW	3051	ev_embeddable_backends (void) EV_NOEXCEPT
2588	{	3052	{
2589	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;	3053	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT | EVBACKEND_IOURING;
2590		3054
2591	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */	3055	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */
2592	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */	3056	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */
2593	flags &= ~EVBACKEND_EPOLL;	3057	flags &= ~EVBACKEND_EPOLL;
2594		3058
		3059	/* EVBACKEND_LINUXAIO is theoretically embeddable, but suffers from a performance overhead */
		3060
2595	return flags;	3061	return flags;
2596	}	3062	}
2597		3063
2598	unsigned int	3064	unsigned int
2599	ev_backend (EV_P) EV_THROW	3065	ev_backend (EV_P) EV_NOEXCEPT
2600	{	3066	{
2601	return backend;	3067	return backend;
2602	}	3068	}
2603		3069
2604	#if EV_FEATURE_API	3070	#if EV_FEATURE_API
2605	unsigned int	3071	unsigned int
2606	ev_iteration (EV_P) EV_THROW	3072	ev_iteration (EV_P) EV_NOEXCEPT
2607	{	3073	{
2608	return loop_count;	3074	return loop_count;
2609	}	3075	}
2610		3076
2611	unsigned int	3077	unsigned int
2612	ev_depth (EV_P) EV_THROW	3078	ev_depth (EV_P) EV_NOEXCEPT
2613	{	3079	{
2614	return loop_depth;	3080	return loop_depth;
2615	}	3081	}
2616		3082
2617	void	3083	void
2618	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	3084	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2619	{	3085	{
2620	io_blocktime = interval;	3086	io_blocktime = interval;
2621	}	3087	}
2622		3088
2623	void	3089	void
2624	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	3090	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2625	{	3091	{
2626	timeout_blocktime = interval;	3092	timeout_blocktime = interval;
2627	}	3093	}
2628		3094
2629	void	3095	void
2630	ev_set_userdata (EV_P_ void *data) EV_THROW	3096	ev_set_userdata (EV_P_ void *data) EV_NOEXCEPT
2631	{	3097	{
2632	userdata = data;	3098	userdata = data;
2633	}	3099	}
2634		3100
2635	void *	3101	void *
2636	ev_userdata (EV_P) EV_THROW	3102	ev_userdata (EV_P) EV_NOEXCEPT
2637	{	3103	{
2638	return userdata;	3104	return userdata;
2639	}	3105	}
2640		3106
2641	void	3107	void
2642	ev_set_invoke_pending_cb (EV_P_ ev_loop_callback invoke_pending_cb) EV_THROW	3108	ev_set_invoke_pending_cb (EV_P_ ev_loop_callback invoke_pending_cb) EV_NOEXCEPT
2643	{	3109	{
2644	invoke_cb = invoke_pending_cb;	3110	invoke_cb = invoke_pending_cb;
2645	}	3111	}
2646		3112
2647	void	3113	void
2648	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_THROW, void (*acquire)(EV_P) EV_THROW) EV_THROW	3114	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_NOEXCEPT, void (*acquire)(EV_P) EV_NOEXCEPT) EV_NOEXCEPT
2649	{	3115	{
2650	release_cb = release;	3116	release_cb = release;
2651	acquire_cb = acquire;	3117	acquire_cb = acquire;
2652	}	3118	}
2653	#endif	3119	#endif
2654		3120
2655	/* initialise a loop structure, must be zero-initialised */	3121	/* initialise a loop structure, must be zero-initialised */
2656	static void noinline ecb_cold	3122	ecb_noinline ecb_cold
		3123	static void
2657	loop_init (EV_P_ unsigned int flags) EV_THROW	3124	loop_init (EV_P_ unsigned int flags) EV_NOEXCEPT
2658	{	3125	{
2659	if (!backend)	3126	if (!backend)
2660	{	3127	{
2661	origflags = flags;	3128	origflags = flags;
2662		3129
…		…
2715	fs_fd = flags & EVFLAG_NOINOTIFY ? -1 : -2;	3182	fs_fd = flags & EVFLAG_NOINOTIFY ? -1 : -2;
2716	#endif	3183	#endif
2717	#if EV_USE_SIGNALFD	3184	#if EV_USE_SIGNALFD
2718	sigfd = flags & EVFLAG_SIGNALFD ? -2 : -1;	3185	sigfd = flags & EVFLAG_SIGNALFD ? -2 : -1;
2719	#endif	3186	#endif
		3187	#if EV_USE_TIMERFD
		3188	timerfd = flags & EVFLAG_NOTIMERFD ? -1 : -2;
		3189	#endif
2720		3190
2721	if (!(flags & EVBACKEND_MASK))	3191	if (!(flags & EVBACKEND_MASK))
2722	flags |= ev_recommended_backends ();	3192	flags |= ev_recommended_backends ();
2723		3193
2724	#if EV_USE_IOCP	3194	#if EV_USE_IOCP
2725	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);	3195	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);
2726	#endif	3196	#endif
2727	#if EV_USE_PORT	3197	#if EV_USE_PORT
2728	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);	3198	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);
2729	#endif	3199	#endif
2730	#if EV_USE_KQUEUE	3200	#if EV_USE_KQUEUE
2731	if (!backend && (flags & EVBACKEND_KQUEUE)) backend = kqueue_init (EV_A_ flags);	3201	if (!backend && (flags & EVBACKEND_KQUEUE )) backend = kqueue_init (EV_A_ flags);
		3202	#endif
		3203	#if EV_USE_IOURING
		3204	if (!backend && (flags & EVBACKEND_IOURING )) backend = iouring_init (EV_A_ flags);
		3205	#endif
		3206	#if EV_USE_LINUXAIO
		3207	if (!backend && (flags & EVBACKEND_LINUXAIO)) backend = linuxaio_init (EV_A_ flags);
2732	#endif	3208	#endif
2733	#if EV_USE_EPOLL	3209	#if EV_USE_EPOLL
2734	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);	3210	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);
2735	#endif	3211	#endif
2736	#if EV_USE_POLL	3212	#if EV_USE_POLL
2737	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);	3213	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);
2738	#endif	3214	#endif
2739	#if EV_USE_SELECT	3215	#if EV_USE_SELECT
2740	if (!backend && (flags & EVBACKEND_SELECT)) backend = select_init (EV_A_ flags);	3216	if (!backend && (flags & EVBACKEND_SELECT )) backend = select_init (EV_A_ flags);
2741	#endif	3217	#endif
2742		3218
2743	ev_prepare_init (&pending_w, pendingcb);	3219	ev_prepare_init (&pending_w, pendingcb);
2744		3220
2745	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	3221	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
…		…
2748	#endif	3224	#endif
2749	}	3225	}
2750	}	3226	}
2751		3227
2752	/* free up a loop structure */	3228	/* free up a loop structure */
2753	void ecb_cold	3229	ecb_cold
		3230	void
2754	ev_loop_destroy (EV_P)	3231	ev_loop_destroy (EV_P)
2755	{	3232	{
2756	int i;	3233	int i;
2757		3234
2758	#if EV_MULTIPLICITY	3235	#if EV_MULTIPLICITY
…		…
2761	return;	3238	return;
2762	#endif	3239	#endif
2763		3240
2764	#if EV_CLEANUP_ENABLE	3241	#if EV_CLEANUP_ENABLE
2765	/* queue cleanup watchers (and execute them) */	3242	/* queue cleanup watchers (and execute them) */
2766	if (expect_false (cleanupcnt))	3243	if (ecb_expect_false (cleanupcnt))
2767	{	3244	{
2768	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);	3245	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);
2769	EV_INVOKE_PENDING;	3246	EV_INVOKE_PENDING;
2770	}	3247	}
2771	#endif	3248	#endif
…		…
2790	#if EV_USE_SIGNALFD	3267	#if EV_USE_SIGNALFD
2791	if (ev_is_active (&sigfd_w))	3268	if (ev_is_active (&sigfd_w))
2792	close (sigfd);	3269	close (sigfd);
2793	#endif	3270	#endif
2794		3271
		3272	#if EV_USE_TIMERFD
		3273	if (ev_is_active (&timerfd_w))
		3274	close (timerfd);
		3275	#endif
		3276
2795	#if EV_USE_INOTIFY	3277	#if EV_USE_INOTIFY
2796	if (fs_fd >= 0)	3278	if (fs_fd >= 0)
2797	close (fs_fd);	3279	close (fs_fd);
2798	#endif	3280	#endif
2799		3281
2800	if (backend_fd >= 0)	3282	if (backend_fd >= 0)
2801	close (backend_fd);	3283	close (backend_fd);
2802		3284
2803	#if EV_USE_IOCP	3285	#if EV_USE_IOCP
2804	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);	3286	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);
2805	#endif	3287	#endif
2806	#if EV_USE_PORT	3288	#if EV_USE_PORT
2807	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);	3289	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);
2808	#endif	3290	#endif
2809	#if EV_USE_KQUEUE	3291	#if EV_USE_KQUEUE
2810	if (backend == EVBACKEND_KQUEUE) kqueue_destroy (EV_A);	3292	if (backend == EVBACKEND_KQUEUE ) kqueue_destroy (EV_A);
		3293	#endif
		3294	#if EV_USE_IOURING
		3295	if (backend == EVBACKEND_IOURING ) iouring_destroy (EV_A);
		3296	#endif
		3297	#if EV_USE_LINUXAIO
		3298	if (backend == EVBACKEND_LINUXAIO) linuxaio_destroy (EV_A);
2811	#endif	3299	#endif
2812	#if EV_USE_EPOLL	3300	#if EV_USE_EPOLL
2813	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);	3301	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);
2814	#endif	3302	#endif
2815	#if EV_USE_POLL	3303	#if EV_USE_POLL
2816	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);	3304	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);
2817	#endif	3305	#endif
2818	#if EV_USE_SELECT	3306	#if EV_USE_SELECT
2819	if (backend == EVBACKEND_SELECT) select_destroy (EV_A);	3307	if (backend == EVBACKEND_SELECT ) select_destroy (EV_A);
2820	#endif	3308	#endif
2821		3309
2822	for (i = NUMPRI; i--; )	3310	for (i = NUMPRI; i--; )
2823	{	3311	{
2824	array_free (pending, [i]);	3312	array_free (pending, [i]);
…		…
2866		3354
2867	inline_size void	3355	inline_size void
2868	loop_fork (EV_P)	3356	loop_fork (EV_P)
2869	{	3357	{
2870	#if EV_USE_PORT	3358	#if EV_USE_PORT
2871	if (backend == EVBACKEND_PORT ) port_fork (EV_A);	3359	if (backend == EVBACKEND_PORT ) port_fork (EV_A);
2872	#endif	3360	#endif
2873	#if EV_USE_KQUEUE	3361	#if EV_USE_KQUEUE
2874	if (backend == EVBACKEND_KQUEUE) kqueue_fork (EV_A);	3362	if (backend == EVBACKEND_KQUEUE ) kqueue_fork (EV_A);
		3363	#endif
		3364	#if EV_USE_IOURING
		3365	if (backend == EVBACKEND_IOURING ) iouring_fork (EV_A);
		3366	#endif
		3367	#if EV_USE_LINUXAIO
		3368	if (backend == EVBACKEND_LINUXAIO) linuxaio_fork (EV_A);
2875	#endif	3369	#endif
2876	#if EV_USE_EPOLL	3370	#if EV_USE_EPOLL
2877	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);	3371	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);
2878	#endif	3372	#endif
2879	#if EV_USE_INOTIFY	3373	#if EV_USE_INOTIFY
2880	infy_fork (EV_A);	3374	infy_fork (EV_A);
2881	#endif	3375	#endif
2882		3376
		3377	if (postfork != 2)
		3378	{
		3379	#if EV_USE_SIGNALFD
		3380	/* surprisingly, nothing needs to be done for signalfd, accoridng to docs, it does the right thing on fork */
		3381	#endif
		3382
		3383	#if EV_USE_TIMERFD
		3384	if (ev_is_active (&timerfd_w))
		3385	{
		3386	ev_ref (EV_A);
		3387	ev_io_stop (EV_A_ &timerfd_w);
		3388
		3389	close (timerfd);
		3390	timerfd = -2;
		3391
		3392	evtimerfd_init (EV_A);
		3393	/* reschedule periodics, in case we missed something */
		3394	ev_feed_event (EV_A_ &timerfd_w, EV_CUSTOM);
		3395	}
		3396	#endif
		3397
2883	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	3398	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2884	if (ev_is_active (&pipe_w))	3399	if (ev_is_active (&pipe_w))
2885	{	3400	{
2886	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */	3401	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */
2887		3402
2888	ev_ref (EV_A);	3403	ev_ref (EV_A);
2889	ev_io_stop (EV_A_ &pipe_w);	3404	ev_io_stop (EV_A_ &pipe_w);
2890		3405
2891	if (evpipe [0] >= 0)	3406	if (evpipe [0] >= 0)
2892	EV_WIN32_CLOSE_FD (evpipe [0]);	3407	EV_WIN32_CLOSE_FD (evpipe [0]);
2893		3408
2894	evpipe_init (EV_A);	3409	evpipe_init (EV_A);
2895	/* iterate over everything, in case we missed something before */	3410	/* iterate over everything, in case we missed something before */
2896	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);	3411	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);
		3412	}
		3413	#endif
2897	}	3414	}
2898	#endif
2899		3415
2900	postfork = 0;	3416	postfork = 0;
2901	}	3417	}
2902		3418
2903	#if EV_MULTIPLICITY	3419	#if EV_MULTIPLICITY
2904		3420
		3421	ecb_cold
2905	struct ev_loop * ecb_cold	3422	struct ev_loop *
2906	ev_loop_new (unsigned int flags) EV_THROW	3423	ev_loop_new (unsigned int flags) EV_NOEXCEPT
2907	{	3424	{
2908	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));	3425	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));
2909		3426
2910	memset (EV_A, 0, sizeof (struct ev_loop));	3427	memset (EV_A, 0, sizeof (struct ev_loop));
2911	loop_init (EV_A_ flags);	3428	loop_init (EV_A_ flags);
…		…
2918	}	3435	}
2919		3436
2920	#endif /* multiplicity */	3437	#endif /* multiplicity */
2921		3438
2922	#if EV_VERIFY	3439	#if EV_VERIFY
2923	static void noinline ecb_cold	3440	ecb_noinline ecb_cold
		3441	static void
2924	verify_watcher (EV_P_ W w)	3442	verify_watcher (EV_P_ W w)
2925	{	3443	{
2926	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));	3444	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));
2927		3445
2928	if (w->pending)	3446	if (w->pending)
2929	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));	3447	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));
2930	}	3448	}
2931		3449
2932	static void noinline ecb_cold	3450	ecb_noinline ecb_cold
		3451	static void
2933	verify_heap (EV_P_ ANHE *heap, int N)	3452	verify_heap (EV_P_ ANHE *heap, int N)
2934	{	3453	{
2935	int i;	3454	int i;
2936		3455
2937	for (i = HEAP0; i < N + HEAP0; ++i)	3456	for (i = HEAP0; i < N + HEAP0; ++i)
…		…
2942		3461
2943	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));	3462	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));
2944	}	3463	}
2945	}	3464	}
2946		3465
2947	static void noinline ecb_cold	3466	ecb_noinline ecb_cold
		3467	static void
2948	array_verify (EV_P_ W *ws, int cnt)	3468	array_verify (EV_P_ W *ws, int cnt)
2949	{	3469	{
2950	while (cnt--)	3470	while (cnt--)
2951	{	3471	{
2952	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));	3472	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));
…		…
2955	}	3475	}
2956	#endif	3476	#endif
2957		3477
2958	#if EV_FEATURE_API	3478	#if EV_FEATURE_API
2959	void ecb_cold	3479	void ecb_cold
2960	ev_verify (EV_P) EV_THROW	3480	ev_verify (EV_P) EV_NOEXCEPT
2961	{	3481	{
2962	#if EV_VERIFY	3482	#if EV_VERIFY
2963	int i;	3483	int i;
2964	WL w, w2;	3484	WL w, w2;
2965		3485
…		…
3041	#endif	3561	#endif
3042	}	3562	}
3043	#endif	3563	#endif
3044		3564
3045	#if EV_MULTIPLICITY	3565	#if EV_MULTIPLICITY
		3566	ecb_cold
3046	struct ev_loop * ecb_cold	3567	struct ev_loop *
3047	#else	3568	#else
3048	int	3569	int
3049	#endif	3570	#endif
3050	ev_default_loop (unsigned int flags) EV_THROW	3571	ev_default_loop (unsigned int flags) EV_NOEXCEPT
3051	{	3572	{
3052	if (!ev_default_loop_ptr)	3573	if (!ev_default_loop_ptr)
3053	{	3574	{
3054	#if EV_MULTIPLICITY	3575	#if EV_MULTIPLICITY
3055	EV_P = ev_default_loop_ptr = &default_loop_struct;	3576	EV_P = ev_default_loop_ptr = &default_loop_struct;
…		…
3074		3595
3075	return ev_default_loop_ptr;	3596	return ev_default_loop_ptr;
3076	}	3597	}
3077		3598
3078	void	3599	void
3079	ev_loop_fork (EV_P) EV_THROW	3600	ev_loop_fork (EV_P) EV_NOEXCEPT
3080	{	3601	{
3081	postfork = 1;	3602	postfork = 1;
3082	}	3603	}
3083		3604
3084	/*****************************************************************************/	3605	/*****************************************************************************/
…		…
3088	{	3609	{
3089	EV_CB_INVOKE ((W)w, revents);	3610	EV_CB_INVOKE ((W)w, revents);
3090	}	3611	}
3091		3612
3092	unsigned int	3613	unsigned int
3093	ev_pending_count (EV_P) EV_THROW	3614	ev_pending_count (EV_P) EV_NOEXCEPT
3094	{	3615	{
3095	int pri;	3616	int pri;
3096	unsigned int count = 0;	3617	unsigned int count = 0;
3097		3618
3098	for (pri = NUMPRI; pri--; )	3619	for (pri = NUMPRI; pri--; )
3099	count += pendingcnt [pri];	3620	count += pendingcnt [pri];
3100		3621
3101	return count;	3622	return count;
3102	}	3623	}
3103		3624
3104	void noinline	3625	ecb_noinline
		3626	void
3105	ev_invoke_pending (EV_P)	3627	ev_invoke_pending (EV_P)
3106	{	3628	{
3107	pendingpri = NUMPRI;	3629	pendingpri = NUMPRI;
3108		3630
3109	while (pendingpri) /* pendingpri possibly gets modified in the inner loop */	3631	do
3110	{	3632	{
3111	--pendingpri;	3633	--pendingpri;
3112		3634
		3635	/* pendingpri possibly gets modified in the inner loop */
3113	while (pendingcnt [pendingpri])	3636	while (pendingcnt [pendingpri])
3114	{	3637	{
3115	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];	3638	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];
3116		3639
3117	p->w->pending = 0;	3640	p->w->pending = 0;
3118	EV_CB_INVOKE (p->w, p->events);	3641	EV_CB_INVOKE (p->w, p->events);
3119	EV_FREQUENT_CHECK;	3642	EV_FREQUENT_CHECK;
3120	}	3643	}
3121	}	3644	}
		3645	while (pendingpri);
3122	}	3646	}
3123		3647
3124	#if EV_IDLE_ENABLE	3648	#if EV_IDLE_ENABLE
3125	/* make idle watchers pending. this handles the "call-idle */	3649	/* make idle watchers pending. this handles the "call-idle */
3126	/* only when higher priorities are idle" logic */	3650	/* only when higher priorities are idle" logic */
3127	inline_size void	3651	inline_size void
3128	idle_reify (EV_P)	3652	idle_reify (EV_P)
3129	{	3653	{
3130	if (expect_false (idleall))	3654	if (ecb_expect_false (idleall))
3131	{	3655	{
3132	int pri;	3656	int pri;
3133		3657
3134	for (pri = NUMPRI; pri--; )	3658	for (pri = NUMPRI; pri--; )
3135	{	3659	{
…		…
3165	{	3689	{
3166	ev_at (w) += w->repeat;	3690	ev_at (w) += w->repeat;
3167	if (ev_at (w) < mn_now)	3691	if (ev_at (w) < mn_now)
3168	ev_at (w) = mn_now;	3692	ev_at (w) = mn_now;
3169		3693
3170	assert (("libev: negative ev_timer repeat value found while processing timers", w->repeat > 0.));	3694	assert (("libev: negative ev_timer repeat value found while processing timers", w->repeat > EV_TS_CONST (0.)));
3171		3695
3172	ANHE_at_cache (timers [HEAP0]);	3696	ANHE_at_cache (timers [HEAP0]);
3173	downheap (timers, timercnt, HEAP0);	3697	downheap (timers, timercnt, HEAP0);
3174	}	3698	}
3175	else	3699	else
…		…
3184	}	3708	}
3185	}	3709	}
3186		3710
3187	#if EV_PERIODIC_ENABLE	3711	#if EV_PERIODIC_ENABLE
3188		3712
3189	static void noinline	3713	ecb_noinline
		3714	static void
3190	periodic_recalc (EV_P_ ev_periodic *w)	3715	periodic_recalc (EV_P_ ev_periodic *w)
3191	{	3716	{
3192	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;	3717	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;
3193	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);	3718	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);
3194		3719
…		…
3196	while (at <= ev_rt_now)	3721	while (at <= ev_rt_now)
3197	{	3722	{
3198	ev_tstamp nat = at + w->interval;	3723	ev_tstamp nat = at + w->interval;
3199		3724
3200	/* when resolution fails us, we use ev_rt_now */	3725	/* when resolution fails us, we use ev_rt_now */
3201	if (expect_false (nat == at))	3726	if (ecb_expect_false (nat == at))
3202	{	3727	{
3203	at = ev_rt_now;	3728	at = ev_rt_now;
3204	break;	3729	break;
3205	}	3730	}
3206		3731
…		…
3252	}	3777	}
3253	}	3778	}
3254		3779
3255	/* simply recalculate all periodics */	3780	/* simply recalculate all periodics */
3256	/* TODO: maybe ensure that at least one event happens when jumping forward? */	3781	/* TODO: maybe ensure that at least one event happens when jumping forward? */
3257	static void noinline ecb_cold	3782	ecb_noinline ecb_cold
		3783	static void
3258	periodics_reschedule (EV_P)	3784	periodics_reschedule (EV_P)
3259	{	3785	{
3260	int i;	3786	int i;
3261		3787
3262	/* adjust periodics after time jump */	3788	/* adjust periodics after time jump */
…		…
3275	reheap (periodics, periodiccnt);	3801	reheap (periodics, periodiccnt);
3276	}	3802	}
3277	#endif	3803	#endif
3278		3804
3279	/* adjust all timers by a given offset */	3805	/* adjust all timers by a given offset */
3280	static void noinline ecb_cold	3806	ecb_noinline ecb_cold
		3807	static void
3281	timers_reschedule (EV_P_ ev_tstamp adjust)	3808	timers_reschedule (EV_P_ ev_tstamp adjust)
3282	{	3809	{
3283	int i;	3810	int i;
3284		3811
3285	for (i = 0; i < timercnt; ++i)	3812	for (i = 0; i < timercnt; ++i)
…		…
3294	/* also detect if there was a timejump, and act accordingly */	3821	/* also detect if there was a timejump, and act accordingly */
3295	inline_speed void	3822	inline_speed void
3296	time_update (EV_P_ ev_tstamp max_block)	3823	time_update (EV_P_ ev_tstamp max_block)
3297	{	3824	{
3298	#if EV_USE_MONOTONIC	3825	#if EV_USE_MONOTONIC
3299	if (expect_true (have_monotonic))	3826	if (ecb_expect_true (have_monotonic))
3300	{	3827	{
3301	int i;	3828	int i;
3302	ev_tstamp odiff = rtmn_diff;	3829	ev_tstamp odiff = rtmn_diff;
3303		3830
3304	mn_now = get_clock ();	3831	mn_now = get_clock ();
3305		3832
3306	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */	3833	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */
3307	/* interpolate in the meantime */	3834	/* interpolate in the meantime */
3308	if (expect_true (mn_now - now_floor < MIN_TIMEJUMP * .5))	3835	if (ecb_expect_true (mn_now - now_floor < EV_TS_CONST (MIN_TIMEJUMP * .5)))
3309	{	3836	{
3310	ev_rt_now = rtmn_diff + mn_now;	3837	ev_rt_now = rtmn_diff + mn_now;
3311	return;	3838	return;
3312	}	3839	}
3313		3840
…		…
3327	ev_tstamp diff;	3854	ev_tstamp diff;
3328	rtmn_diff = ev_rt_now - mn_now;	3855	rtmn_diff = ev_rt_now - mn_now;
3329		3856
3330	diff = odiff - rtmn_diff;	3857	diff = odiff - rtmn_diff;
3331		3858
3332	if (expect_true ((diff < 0. ? -diff : diff) < MIN_TIMEJUMP))	3859	if (ecb_expect_true ((diff < EV_TS_CONST (0.) ? -diff : diff) < EV_TS_CONST (MIN_TIMEJUMP)))
3333	return; /* all is well */	3860	return; /* all is well */
3334		3861
3335	ev_rt_now = ev_time ();	3862	ev_rt_now = ev_time ();
3336	mn_now = get_clock ();	3863	mn_now = get_clock ();
3337	now_floor = mn_now;	3864	now_floor = mn_now;
…		…
3346	else	3873	else
3347	#endif	3874	#endif
3348	{	3875	{
3349	ev_rt_now = ev_time ();	3876	ev_rt_now = ev_time ();
3350		3877
3351	if (expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + MIN_TIMEJUMP))	3878	if (ecb_expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + EV_TS_CONST (MIN_TIMEJUMP)))
3352	{	3879	{
3353	/* adjust timers. this is easy, as the offset is the same for all of them */	3880	/* adjust timers. this is easy, as the offset is the same for all of them */
3354	timers_reschedule (EV_A_ ev_rt_now - mn_now);	3881	timers_reschedule (EV_A_ ev_rt_now - mn_now);
3355	#if EV_PERIODIC_ENABLE	3882	#if EV_PERIODIC_ENABLE
3356	periodics_reschedule (EV_A);	3883	periodics_reschedule (EV_A);
…		…
3379	#if EV_VERIFY >= 2	3906	#if EV_VERIFY >= 2
3380	ev_verify (EV_A);	3907	ev_verify (EV_A);
3381	#endif	3908	#endif
3382		3909
3383	#ifndef _WIN32	3910	#ifndef _WIN32
3384	if (expect_false (curpid)) /* penalise the forking check even more */	3911	if (ecb_expect_false (curpid)) /* penalise the forking check even more */
3385	if (expect_false (getpid () != curpid))	3912	if (ecb_expect_false (getpid () != curpid))
3386	{	3913	{
3387	curpid = getpid ();	3914	curpid = getpid ();
3388	postfork = 1;	3915	postfork = 1;
3389	}	3916	}
3390	#endif	3917	#endif
3391		3918
3392	#if EV_FORK_ENABLE	3919	#if EV_FORK_ENABLE
3393	/* we might have forked, so queue fork handlers */	3920	/* we might have forked, so queue fork handlers */
3394	if (expect_false (postfork))	3921	if (ecb_expect_false (postfork))
3395	if (forkcnt)	3922	if (forkcnt)
3396	{	3923	{
3397	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);	3924	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);
3398	EV_INVOKE_PENDING;	3925	EV_INVOKE_PENDING;
3399	}	3926	}
3400	#endif	3927	#endif
3401		3928
3402	#if EV_PREPARE_ENABLE	3929	#if EV_PREPARE_ENABLE
3403	/* queue prepare watchers (and execute them) */	3930	/* queue prepare watchers (and execute them) */
3404	if (expect_false (preparecnt))	3931	if (ecb_expect_false (preparecnt))
3405	{	3932	{
3406	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);	3933	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);
3407	EV_INVOKE_PENDING;	3934	EV_INVOKE_PENDING;
3408	}	3935	}
3409	#endif	3936	#endif
3410		3937
3411	if (expect_false (loop_done))	3938	if (ecb_expect_false (loop_done))
3412	break;	3939	break;
3413		3940
3414	/* we might have forked, so reify kernel state if necessary */	3941	/* we might have forked, so reify kernel state if necessary */
3415	if (expect_false (postfork))	3942	if (ecb_expect_false (postfork))
3416	loop_fork (EV_A);	3943	loop_fork (EV_A);
3417		3944
3418	/* update fd-related kernel structures */	3945	/* update fd-related kernel structures */
3419	fd_reify (EV_A);	3946	fd_reify (EV_A);
3420		3947
…		…
3425		3952
3426	/* remember old timestamp for io_blocktime calculation */	3953	/* remember old timestamp for io_blocktime calculation */
3427	ev_tstamp prev_mn_now = mn_now;	3954	ev_tstamp prev_mn_now = mn_now;
3428		3955
3429	/* update time to cancel out callback processing overhead */	3956	/* update time to cancel out callback processing overhead */
3430	time_update (EV_A_ 1e100);	3957	time_update (EV_A_ EV_TS_CONST (EV_TSTAMP_HUGE));
3431		3958
3432	/* from now on, we want a pipe-wake-up */	3959	/* from now on, we want a pipe-wake-up */
3433	pipe_write_wanted = 1;	3960	pipe_write_wanted = 1;
3434		3961
3435	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */	3962	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */
3436		3963
3437	if (expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))	3964	if (ecb_expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))
3438	{	3965	{
3439	waittime = MAX_BLOCKTIME;	3966	waittime = EV_TS_CONST (MAX_BLOCKTIME);
3440		3967
3441	if (timercnt)	3968	if (timercnt)
3442	{	3969	{
3443	ev_tstamp to = ANHE_at (timers [HEAP0]) - mn_now;	3970	ev_tstamp to = ANHE_at (timers [HEAP0]) - mn_now;
3444	if (waittime > to) waittime = to;	3971	if (waittime > to) waittime = to;
…		…
3451	if (waittime > to) waittime = to;	3978	if (waittime > to) waittime = to;
3452	}	3979	}
3453	#endif	3980	#endif
3454		3981
3455	/* don't let timeouts decrease the waittime below timeout_blocktime */	3982	/* don't let timeouts decrease the waittime below timeout_blocktime */
3456	if (expect_false (waittime < timeout_blocktime))	3983	if (ecb_expect_false (waittime < timeout_blocktime))
3457	waittime = timeout_blocktime;	3984	waittime = timeout_blocktime;
3458		3985
3459	/* at this point, we NEED to wait, so we have to ensure */	3986	/* now there are two more special cases left, either we have
3460	/* to pass a minimum nonzero value to the backend */	3987	* already-expired timers, so we should not sleep, or we have timers
		3988	* that expire very soon, in which case we need to wait for a minimum
		3989	* amount of time for some event loop backends.
		3990	*/
3461	if (expect_false (waittime < backend_mintime))	3991	if (ecb_expect_false (waittime < backend_mintime))
		3992	waittime = waittime <= EV_TS_CONST (0.)
		3993	? EV_TS_CONST (0.)
3462	waittime = backend_mintime;	3994	: backend_mintime;
3463		3995
3464	/* extra check because io_blocktime is commonly 0 */	3996	/* extra check because io_blocktime is commonly 0 */
3465	if (expect_false (io_blocktime))	3997	if (ecb_expect_false (io_blocktime))
3466	{	3998	{
3467	sleeptime = io_blocktime - (mn_now - prev_mn_now);	3999	sleeptime = io_blocktime - (mn_now - prev_mn_now);
3468		4000
3469	if (sleeptime > waittime - backend_mintime)	4001	if (sleeptime > waittime - backend_mintime)
3470	sleeptime = waittime - backend_mintime;	4002	sleeptime = waittime - backend_mintime;
3471		4003
3472	if (expect_true (sleeptime > 0.))	4004	if (ecb_expect_true (sleeptime > EV_TS_CONST (0.)))
3473	{	4005	{
3474	ev_sleep (sleeptime);	4006	ev_sleep (sleeptime);
3475	waittime -= sleeptime;	4007	waittime -= sleeptime;
3476	}	4008	}
3477	}	4009	}
…		…
3491	{	4023	{
3492	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));	4024	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));
3493	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);	4025	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);
3494	}	4026	}
3495		4027
3496
3497	/* update ev_rt_now, do magic */	4028	/* update ev_rt_now, do magic */
3498	time_update (EV_A_ waittime + sleeptime);	4029	time_update (EV_A_ waittime + sleeptime);
3499	}	4030	}
3500		4031
3501	/* queue pending timers and reschedule them */	4032	/* queue pending timers and reschedule them */
…		…
3509	idle_reify (EV_A);	4040	idle_reify (EV_A);
3510	#endif	4041	#endif
3511		4042
3512	#if EV_CHECK_ENABLE	4043	#if EV_CHECK_ENABLE
3513	/* queue check watchers, to be executed first */	4044	/* queue check watchers, to be executed first */
3514	if (expect_false (checkcnt))	4045	if (ecb_expect_false (checkcnt))
3515	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);	4046	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);
3516	#endif	4047	#endif
3517		4048
3518	EV_INVOKE_PENDING;	4049	EV_INVOKE_PENDING;
3519	}	4050	}
3520	while (expect_true (	4051	while (ecb_expect_true (
3521	activecnt	4052	activecnt
3522	&& !loop_done	4053	&& !loop_done
3523	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))	4054	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))
3524	));	4055	));
3525		4056
…		…
3532		4063
3533	return activecnt;	4064	return activecnt;
3534	}	4065	}
3535		4066
3536	void	4067	void
3537	ev_break (EV_P_ int how) EV_THROW	4068	ev_break (EV_P_ int how) EV_NOEXCEPT
3538	{	4069	{
3539	loop_done = how;	4070	loop_done = how;
3540	}	4071	}
3541		4072
3542	void	4073	void
3543	ev_ref (EV_P) EV_THROW	4074	ev_ref (EV_P) EV_NOEXCEPT
3544	{	4075	{
3545	++activecnt;	4076	++activecnt;
3546	}	4077	}
3547		4078
3548	void	4079	void
3549	ev_unref (EV_P) EV_THROW	4080	ev_unref (EV_P) EV_NOEXCEPT
3550	{	4081	{
3551	--activecnt;	4082	--activecnt;
3552	}	4083	}
3553		4084
3554	void	4085	void
3555	ev_now_update (EV_P) EV_THROW	4086	ev_now_update (EV_P) EV_NOEXCEPT
3556	{	4087	{
3557	time_update (EV_A_ 1e100);	4088	time_update (EV_A_ EV_TSTAMP_HUGE);
3558	}	4089	}
3559		4090
3560	void	4091	void
3561	ev_suspend (EV_P) EV_THROW	4092	ev_suspend (EV_P) EV_NOEXCEPT
3562	{	4093	{
3563	ev_now_update (EV_A);	4094	ev_now_update (EV_A);
3564	}	4095	}
3565		4096
3566	void	4097	void
3567	ev_resume (EV_P) EV_THROW	4098	ev_resume (EV_P) EV_NOEXCEPT
3568	{	4099	{
3569	ev_tstamp mn_prev = mn_now;	4100	ev_tstamp mn_prev = mn_now;
3570		4101
3571	ev_now_update (EV_A);	4102	ev_now_update (EV_A);
3572	timers_reschedule (EV_A_ mn_now - mn_prev);	4103	timers_reschedule (EV_A_ mn_now - mn_prev);
…		…
3589	inline_size void	4120	inline_size void
3590	wlist_del (WL *head, WL elem)	4121	wlist_del (WL *head, WL elem)
3591	{	4122	{
3592	while (*head)	4123	while (*head)
3593	{	4124	{
3594	if (expect_true (*head == elem))	4125	if (ecb_expect_true (*head == elem))
3595	{	4126	{
3596	*head = elem->next;	4127	*head = elem->next;
3597	break;	4128	break;
3598	}	4129	}
3599		4130
…		…
3611	w->pending = 0;	4142	w->pending = 0;
3612	}	4143	}
3613	}	4144	}
3614		4145
3615	int	4146	int
3616	ev_clear_pending (EV_P_ void *w) EV_THROW	4147	ev_clear_pending (EV_P_ void *w) EV_NOEXCEPT
3617	{	4148	{
3618	W w_ = (W)w;	4149	W w_ = (W)w;
3619	int pending = w_->pending;	4150	int pending = w_->pending;
3620		4151
3621	if (expect_true (pending))	4152	if (ecb_expect_true (pending))
3622	{	4153	{
3623	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;	4154	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;
3624	p->w = (W)&pending_w;	4155	p->w = (W)&pending_w;
3625	w_->pending = 0;	4156	w_->pending = 0;
3626	return p->events;	4157	return p->events;
…		…
3653	w->active = 0;	4184	w->active = 0;
3654	}	4185	}
3655		4186
3656	/*****************************************************************************/	4187	/*****************************************************************************/
3657		4188
3658	void noinline	4189	ecb_noinline
		4190	void
3659	ev_io_start (EV_P_ ev_io *w) EV_THROW	4191	ev_io_start (EV_P_ ev_io *w) EV_NOEXCEPT
3660	{	4192	{
3661	int fd = w->fd;	4193	int fd = w->fd;
3662		4194
3663	if (expect_false (ev_is_active (w)))	4195	if (ecb_expect_false (ev_is_active (w)))
3664	return;	4196	return;
3665		4197
3666	assert (("libev: ev_io_start called with negative fd", fd >= 0));	4198	assert (("libev: ev_io_start called with negative fd", fd >= 0));
3667	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));	4199	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));
3668		4200
		4201	#if EV_VERIFY >= 2
		4202	assert (("libev: ev_io_start called on watcher with invalid fd", fd_valid (fd)));
		4203	#endif
3669	EV_FREQUENT_CHECK;	4204	EV_FREQUENT_CHECK;
3670		4205
3671	ev_start (EV_A_ (W)w, 1);	4206	ev_start (EV_A_ (W)w, 1);
3672	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_init_zero);	4207	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_needsize_zerofill);
3673	wlist_add (&anfds[fd].head, (WL)w);	4208	wlist_add (&anfds[fd].head, (WL)w);
3674		4209
3675	/* common bug, apparently */	4210	/* common bug, apparently */
3676	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));	4211	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));
3677		4212
…		…
3679	w->events &= ~EV__IOFDSET;	4214	w->events &= ~EV__IOFDSET;
3680		4215
3681	EV_FREQUENT_CHECK;	4216	EV_FREQUENT_CHECK;
3682	}	4217	}
3683		4218
3684	void noinline	4219	ecb_noinline
		4220	void
3685	ev_io_stop (EV_P_ ev_io *w) EV_THROW	4221	ev_io_stop (EV_P_ ev_io *w) EV_NOEXCEPT
3686	{	4222	{
3687	clear_pending (EV_A_ (W)w);	4223	clear_pending (EV_A_ (W)w);
3688	if (expect_false (!ev_is_active (w)))	4224	if (ecb_expect_false (!ev_is_active (w)))
3689	return;	4225	return;
3690		4226
3691	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));	4227	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));
3692		4228
		4229	#if EV_VERIFY >= 2
		4230	assert (("libev: ev_io_stop called on watcher with invalid fd", fd_valid (w->fd)));
		4231	#endif
3693	EV_FREQUENT_CHECK;	4232	EV_FREQUENT_CHECK;
3694		4233
3695	wlist_del (&anfds[w->fd].head, (WL)w);	4234	wlist_del (&anfds[w->fd].head, (WL)w);
3696	ev_stop (EV_A_ (W)w);	4235	ev_stop (EV_A_ (W)w);
3697		4236
3698	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);	4237	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);
3699		4238
3700	EV_FREQUENT_CHECK;	4239	EV_FREQUENT_CHECK;
3701	}	4240	}
3702		4241
3703	void noinline	4242	ecb_noinline
		4243	void
3704	ev_timer_start (EV_P_ ev_timer *w) EV_THROW	4244	ev_timer_start (EV_P_ ev_timer *w) EV_NOEXCEPT
3705	{	4245	{
3706	if (expect_false (ev_is_active (w)))	4246	if (ecb_expect_false (ev_is_active (w)))
3707	return;	4247	return;
3708		4248
3709	ev_at (w) += mn_now;	4249	ev_at (w) += mn_now;
3710		4250
3711	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));	4251	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));
3712		4252
3713	EV_FREQUENT_CHECK;	4253	EV_FREQUENT_CHECK;
3714		4254
3715	++timercnt;	4255	++timercnt;
3716	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);	4256	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);
3717	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, EMPTY2);	4257	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, array_needsize_noinit);
3718	ANHE_w (timers [ev_active (w)]) = (WT)w;	4258	ANHE_w (timers [ev_active (w)]) = (WT)w;
3719	ANHE_at_cache (timers [ev_active (w)]);	4259	ANHE_at_cache (timers [ev_active (w)]);
3720	upheap (timers, ev_active (w));	4260	upheap (timers, ev_active (w));
3721		4261
3722	EV_FREQUENT_CHECK;	4262	EV_FREQUENT_CHECK;
3723		4263
3724	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/	4264	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/
3725	}	4265	}
3726		4266
3727	void noinline	4267	ecb_noinline
		4268	void
3728	ev_timer_stop (EV_P_ ev_timer *w) EV_THROW	4269	ev_timer_stop (EV_P_ ev_timer *w) EV_NOEXCEPT
3729	{	4270	{
3730	clear_pending (EV_A_ (W)w);	4271	clear_pending (EV_A_ (W)w);
3731	if (expect_false (!ev_is_active (w)))	4272	if (ecb_expect_false (!ev_is_active (w)))
3732	return;	4273	return;
3733		4274
3734	EV_FREQUENT_CHECK;	4275	EV_FREQUENT_CHECK;
3735		4276
3736	{	4277	{
…		…
3738		4279
3739	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));	4280	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));
3740		4281
3741	--timercnt;	4282	--timercnt;
3742		4283
3743	if (expect_true (active < timercnt + HEAP0))	4284	if (ecb_expect_true (active < timercnt + HEAP0))
3744	{	4285	{
3745	timers [active] = timers [timercnt + HEAP0];	4286	timers [active] = timers [timercnt + HEAP0];
3746	adjustheap (timers, timercnt, active);	4287	adjustheap (timers, timercnt, active);
3747	}	4288	}
3748	}	4289	}
…		…
3752	ev_stop (EV_A_ (W)w);	4293	ev_stop (EV_A_ (W)w);
3753		4294
3754	EV_FREQUENT_CHECK;	4295	EV_FREQUENT_CHECK;
3755	}	4296	}
3756		4297
3757	void noinline	4298	ecb_noinline
		4299	void
3758	ev_timer_again (EV_P_ ev_timer *w) EV_THROW	4300	ev_timer_again (EV_P_ ev_timer *w) EV_NOEXCEPT
3759	{	4301	{
3760	EV_FREQUENT_CHECK;	4302	EV_FREQUENT_CHECK;
3761		4303
3762	clear_pending (EV_A_ (W)w);	4304	clear_pending (EV_A_ (W)w);
3763		4305
…		…
3780		4322
3781	EV_FREQUENT_CHECK;	4323	EV_FREQUENT_CHECK;
3782	}	4324	}
3783		4325
3784	ev_tstamp	4326	ev_tstamp
3785	ev_timer_remaining (EV_P_ ev_timer *w) EV_THROW	4327	ev_timer_remaining (EV_P_ ev_timer *w) EV_NOEXCEPT
3786	{	4328	{
3787	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);	4329	return ev_at (w) - (ev_is_active (w) ? mn_now : EV_TS_CONST (0.));
3788	}	4330	}
3789		4331
3790	#if EV_PERIODIC_ENABLE	4332	#if EV_PERIODIC_ENABLE
3791	void noinline	4333	ecb_noinline
		4334	void
3792	ev_periodic_start (EV_P_ ev_periodic *w) EV_THROW	4335	ev_periodic_start (EV_P_ ev_periodic *w) EV_NOEXCEPT
3793	{	4336	{
3794	if (expect_false (ev_is_active (w)))	4337	if (ecb_expect_false (ev_is_active (w)))
3795	return;	4338	return;
		4339
		4340	#if EV_USE_TIMERFD
		4341	if (timerfd == -2)
		4342	evtimerfd_init (EV_A);
		4343	#endif
3796		4344
3797	if (w->reschedule_cb)	4345	if (w->reschedule_cb)
3798	ev_at (w) = w->reschedule_cb (w, ev_rt_now);	4346	ev_at (w) = w->reschedule_cb (w, ev_rt_now);
3799	else if (w->interval)	4347	else if (w->interval)
3800	{	4348	{
…		…
3806		4354
3807	EV_FREQUENT_CHECK;	4355	EV_FREQUENT_CHECK;
3808		4356
3809	++periodiccnt;	4357	++periodiccnt;
3810	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);	4358	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);
3811	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, EMPTY2);	4359	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, array_needsize_noinit);
3812	ANHE_w (periodics [ev_active (w)]) = (WT)w;	4360	ANHE_w (periodics [ev_active (w)]) = (WT)w;
3813	ANHE_at_cache (periodics [ev_active (w)]);	4361	ANHE_at_cache (periodics [ev_active (w)]);
3814	upheap (periodics, ev_active (w));	4362	upheap (periodics, ev_active (w));
3815		4363
3816	EV_FREQUENT_CHECK;	4364	EV_FREQUENT_CHECK;
3817		4365
3818	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/	4366	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/
3819	}	4367	}
3820		4368
3821	void noinline	4369	ecb_noinline
		4370	void
3822	ev_periodic_stop (EV_P_ ev_periodic *w) EV_THROW	4371	ev_periodic_stop (EV_P_ ev_periodic *w) EV_NOEXCEPT
3823	{	4372	{
3824	clear_pending (EV_A_ (W)w);	4373	clear_pending (EV_A_ (W)w);
3825	if (expect_false (!ev_is_active (w)))	4374	if (ecb_expect_false (!ev_is_active (w)))
3826	return;	4375	return;
3827		4376
3828	EV_FREQUENT_CHECK;	4377	EV_FREQUENT_CHECK;
3829		4378
3830	{	4379	{
…		…
3832		4381
3833	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));	4382	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));
3834		4383
3835	--periodiccnt;	4384	--periodiccnt;
3836		4385
3837	if (expect_true (active < periodiccnt + HEAP0))	4386	if (ecb_expect_true (active < periodiccnt + HEAP0))
3838	{	4387	{
3839	periodics [active] = periodics [periodiccnt + HEAP0];	4388	periodics [active] = periodics [periodiccnt + HEAP0];
3840	adjustheap (periodics, periodiccnt, active);	4389	adjustheap (periodics, periodiccnt, active);
3841	}	4390	}
3842	}	4391	}
…		…
3844	ev_stop (EV_A_ (W)w);	4393	ev_stop (EV_A_ (W)w);
3845		4394
3846	EV_FREQUENT_CHECK;	4395	EV_FREQUENT_CHECK;
3847	}	4396	}
3848		4397
3849	void noinline	4398	ecb_noinline
		4399	void
3850	ev_periodic_again (EV_P_ ev_periodic *w) EV_THROW	4400	ev_periodic_again (EV_P_ ev_periodic *w) EV_NOEXCEPT
3851	{	4401	{
3852	/* TODO: use adjustheap and recalculation */	4402	/* TODO: use adjustheap and recalculation */
3853	ev_periodic_stop (EV_A_ w);	4403	ev_periodic_stop (EV_A_ w);
3854	ev_periodic_start (EV_A_ w);	4404	ev_periodic_start (EV_A_ w);
3855	}	4405	}
…		…
3859	# define SA_RESTART 0	4409	# define SA_RESTART 0
3860	#endif	4410	#endif
3861		4411
3862	#if EV_SIGNAL_ENABLE	4412	#if EV_SIGNAL_ENABLE
3863		4413
3864	void noinline	4414	ecb_noinline
		4415	void
3865	ev_signal_start (EV_P_ ev_signal *w) EV_THROW	4416	ev_signal_start (EV_P_ ev_signal *w) EV_NOEXCEPT
3866	{	4417	{
3867	if (expect_false (ev_is_active (w)))	4418	if (ecb_expect_false (ev_is_active (w)))
3868	return;	4419	return;
3869		4420
3870	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));	4421	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));
3871		4422
3872	#if EV_MULTIPLICITY	4423	#if EV_MULTIPLICITY
…		…
3941	}	4492	}
3942		4493
3943	EV_FREQUENT_CHECK;	4494	EV_FREQUENT_CHECK;
3944	}	4495	}
3945		4496
3946	void noinline	4497	ecb_noinline
		4498	void
3947	ev_signal_stop (EV_P_ ev_signal *w) EV_THROW	4499	ev_signal_stop (EV_P_ ev_signal *w) EV_NOEXCEPT
3948	{	4500	{
3949	clear_pending (EV_A_ (W)w);	4501	clear_pending (EV_A_ (W)w);
3950	if (expect_false (!ev_is_active (w)))	4502	if (ecb_expect_false (!ev_is_active (w)))
3951	return;	4503	return;
3952		4504
3953	EV_FREQUENT_CHECK;	4505	EV_FREQUENT_CHECK;
3954		4506
3955	wlist_del (&signals [w->signum - 1].head, (WL)w);	4507	wlist_del (&signals [w->signum - 1].head, (WL)w);
…		…
3983	#endif	4535	#endif
3984		4536
3985	#if EV_CHILD_ENABLE	4537	#if EV_CHILD_ENABLE
3986		4538
3987	void	4539	void
3988	ev_child_start (EV_P_ ev_child *w) EV_THROW	4540	ev_child_start (EV_P_ ev_child *w) EV_NOEXCEPT
3989	{	4541	{
3990	#if EV_MULTIPLICITY	4542	#if EV_MULTIPLICITY
3991	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));	4543	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));
3992	#endif	4544	#endif
3993	if (expect_false (ev_is_active (w)))	4545	if (ecb_expect_false (ev_is_active (w)))
3994	return;	4546	return;
3995		4547
3996	EV_FREQUENT_CHECK;	4548	EV_FREQUENT_CHECK;
3997		4549
3998	ev_start (EV_A_ (W)w, 1);	4550	ev_start (EV_A_ (W)w, 1);
…		…
4000		4552
4001	EV_FREQUENT_CHECK;	4553	EV_FREQUENT_CHECK;
4002	}	4554	}
4003		4555
4004	void	4556	void
4005	ev_child_stop (EV_P_ ev_child *w) EV_THROW	4557	ev_child_stop (EV_P_ ev_child *w) EV_NOEXCEPT
4006	{	4558	{
4007	clear_pending (EV_A_ (W)w);	4559	clear_pending (EV_A_ (W)w);
4008	if (expect_false (!ev_is_active (w)))	4560	if (ecb_expect_false (!ev_is_active (w)))
4009	return;	4561	return;
4010		4562
4011	EV_FREQUENT_CHECK;	4563	EV_FREQUENT_CHECK;
4012		4564
4013	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);	4565	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);
…		…
4027		4579
4028	#define DEF_STAT_INTERVAL 5.0074891	4580	#define DEF_STAT_INTERVAL 5.0074891
4029	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */	4581	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */
4030	#define MIN_STAT_INTERVAL 0.1074891	4582	#define MIN_STAT_INTERVAL 0.1074891
4031		4583
4032	static void noinline stat_timer_cb (EV_P_ ev_timer *w_, int revents);	4584	ecb_noinline static void stat_timer_cb (EV_P_ ev_timer *w_, int revents);
4033		4585
4034	#if EV_USE_INOTIFY	4586	#if EV_USE_INOTIFY
4035		4587
4036	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */	4588	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */
4037	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)	4589	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)
4038		4590
4039	static void noinline	4591	ecb_noinline
		4592	static void
4040	infy_add (EV_P_ ev_stat *w)	4593	infy_add (EV_P_ ev_stat *w)
4041	{	4594	{
4042	w->wd = inotify_add_watch (fs_fd, w->path,	4595	w->wd = inotify_add_watch (fs_fd, w->path,
4043	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY	4596	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY
4044	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO	4597	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO
…		…
4108	if (ev_is_active (&w->timer)) ev_ref (EV_A);	4661	if (ev_is_active (&w->timer)) ev_ref (EV_A);
4109	ev_timer_again (EV_A_ &w->timer);	4662	ev_timer_again (EV_A_ &w->timer);
4110	if (ev_is_active (&w->timer)) ev_unref (EV_A);	4663	if (ev_is_active (&w->timer)) ev_unref (EV_A);
4111	}	4664	}
4112		4665
4113	static void noinline	4666	ecb_noinline
		4667	static void
4114	infy_del (EV_P_ ev_stat *w)	4668	infy_del (EV_P_ ev_stat *w)
4115	{	4669	{
4116	int slot;	4670	int slot;
4117	int wd = w->wd;	4671	int wd = w->wd;
4118		4672
…		…
4125		4679
4126	/* remove this watcher, if others are watching it, they will rearm */	4680	/* remove this watcher, if others are watching it, they will rearm */
4127	inotify_rm_watch (fs_fd, wd);	4681	inotify_rm_watch (fs_fd, wd);
4128	}	4682	}
4129		4683
4130	static void noinline	4684	ecb_noinline
		4685	static void
4131	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)	4686	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)
4132	{	4687	{
4133	if (slot < 0)	4688	if (slot < 0)
4134	/* overflow, need to check for all hash slots */	4689	/* overflow, need to check for all hash slots */
4135	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)	4690	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)
…		…
4171	infy_wd (EV_A_ ev->wd, ev->wd, ev);	4726	infy_wd (EV_A_ ev->wd, ev->wd, ev);
4172	ofs += sizeof (struct inotify_event) + ev->len;	4727	ofs += sizeof (struct inotify_event) + ev->len;
4173	}	4728	}
4174	}	4729	}
4175		4730
4176	inline_size void ecb_cold	4731	inline_size ecb_cold
		4732	void
4177	ev_check_2625 (EV_P)	4733	ev_check_2625 (EV_P)
4178	{	4734	{
4179	/* kernels < 2.6.25 are borked	4735	/* kernels < 2.6.25 are borked
4180	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html	4736	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html
4181	*/	4737	*/
…		…
4271	#else	4827	#else
4272	# define EV_LSTAT(p,b) lstat (p, b)	4828	# define EV_LSTAT(p,b) lstat (p, b)
4273	#endif	4829	#endif
4274		4830
4275	void	4831	void
4276	ev_stat_stat (EV_P_ ev_stat *w) EV_THROW	4832	ev_stat_stat (EV_P_ ev_stat *w) EV_NOEXCEPT
4277	{	4833	{
4278	if (lstat (w->path, &w->attr) < 0)	4834	if (lstat (w->path, &w->attr) < 0)
4279	w->attr.st_nlink = 0;	4835	w->attr.st_nlink = 0;
4280	else if (!w->attr.st_nlink)	4836	else if (!w->attr.st_nlink)
4281	w->attr.st_nlink = 1;	4837	w->attr.st_nlink = 1;
4282	}	4838	}
4283		4839
4284	static void noinline	4840	ecb_noinline
		4841	static void
4285	stat_timer_cb (EV_P_ ev_timer *w_, int revents)	4842	stat_timer_cb (EV_P_ ev_timer *w_, int revents)
4286	{	4843	{
4287	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));	4844	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));
4288		4845
4289	ev_statdata prev = w->attr;	4846	ev_statdata prev = w->attr;
…		…
4320	ev_feed_event (EV_A_ w, EV_STAT);	4877	ev_feed_event (EV_A_ w, EV_STAT);
4321	}	4878	}
4322	}	4879	}
4323		4880
4324	void	4881	void
4325	ev_stat_start (EV_P_ ev_stat *w) EV_THROW	4882	ev_stat_start (EV_P_ ev_stat *w) EV_NOEXCEPT
4326	{	4883	{
4327	if (expect_false (ev_is_active (w)))	4884	if (ecb_expect_false (ev_is_active (w)))
4328	return;	4885	return;
4329		4886
4330	ev_stat_stat (EV_A_ w);	4887	ev_stat_stat (EV_A_ w);
4331		4888
4332	if (w->interval < MIN_STAT_INTERVAL && w->interval)	4889	if (w->interval < MIN_STAT_INTERVAL && w->interval)
…		…
4351		4908
4352	EV_FREQUENT_CHECK;	4909	EV_FREQUENT_CHECK;
4353	}	4910	}
4354		4911
4355	void	4912	void
4356	ev_stat_stop (EV_P_ ev_stat *w) EV_THROW	4913	ev_stat_stop (EV_P_ ev_stat *w) EV_NOEXCEPT
4357	{	4914	{
4358	clear_pending (EV_A_ (W)w);	4915	clear_pending (EV_A_ (W)w);
4359	if (expect_false (!ev_is_active (w)))	4916	if (ecb_expect_false (!ev_is_active (w)))
4360	return;	4917	return;
4361		4918
4362	EV_FREQUENT_CHECK;	4919	EV_FREQUENT_CHECK;
4363		4920
4364	#if EV_USE_INOTIFY	4921	#if EV_USE_INOTIFY
…		…
4377	}	4934	}
4378	#endif	4935	#endif
4379		4936
4380	#if EV_IDLE_ENABLE	4937	#if EV_IDLE_ENABLE
4381	void	4938	void
4382	ev_idle_start (EV_P_ ev_idle *w) EV_THROW	4939	ev_idle_start (EV_P_ ev_idle *w) EV_NOEXCEPT
4383	{	4940	{
4384	if (expect_false (ev_is_active (w)))	4941	if (ecb_expect_false (ev_is_active (w)))
4385	return;	4942	return;
4386		4943
4387	pri_adjust (EV_A_ (W)w);	4944	pri_adjust (EV_A_ (W)w);
4388		4945
4389	EV_FREQUENT_CHECK;	4946	EV_FREQUENT_CHECK;
…		…
4392	int active = ++idlecnt [ABSPRI (w)];	4949	int active = ++idlecnt [ABSPRI (w)];
4393		4950
4394	++idleall;	4951	++idleall;
4395	ev_start (EV_A_ (W)w, active);	4952	ev_start (EV_A_ (W)w, active);
4396		4953
4397	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, EMPTY2);	4954	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, array_needsize_noinit);
4398	idles [ABSPRI (w)][active - 1] = w;	4955	idles [ABSPRI (w)][active - 1] = w;
4399	}	4956	}
4400		4957
4401	EV_FREQUENT_CHECK;	4958	EV_FREQUENT_CHECK;
4402	}	4959	}
4403		4960
4404	void	4961	void
4405	ev_idle_stop (EV_P_ ev_idle *w) EV_THROW	4962	ev_idle_stop (EV_P_ ev_idle *w) EV_NOEXCEPT
4406	{	4963	{
4407	clear_pending (EV_A_ (W)w);	4964	clear_pending (EV_A_ (W)w);
4408	if (expect_false (!ev_is_active (w)))	4965	if (ecb_expect_false (!ev_is_active (w)))
4409	return;	4966	return;
4410		4967
4411	EV_FREQUENT_CHECK;	4968	EV_FREQUENT_CHECK;
4412		4969
4413	{	4970	{
…		…
4424	}	4981	}
4425	#endif	4982	#endif
4426		4983
4427	#if EV_PREPARE_ENABLE	4984	#if EV_PREPARE_ENABLE
4428	void	4985	void
4429	ev_prepare_start (EV_P_ ev_prepare *w) EV_THROW	4986	ev_prepare_start (EV_P_ ev_prepare *w) EV_NOEXCEPT
4430	{	4987	{
4431	if (expect_false (ev_is_active (w)))	4988	if (ecb_expect_false (ev_is_active (w)))
4432	return;	4989	return;
4433		4990
4434	EV_FREQUENT_CHECK;	4991	EV_FREQUENT_CHECK;
4435		4992
4436	ev_start (EV_A_ (W)w, ++preparecnt);	4993	ev_start (EV_A_ (W)w, ++preparecnt);
4437	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, EMPTY2);	4994	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, array_needsize_noinit);
4438	prepares [preparecnt - 1] = w;	4995	prepares [preparecnt - 1] = w;
4439		4996
4440	EV_FREQUENT_CHECK;	4997	EV_FREQUENT_CHECK;
4441	}	4998	}
4442		4999
4443	void	5000	void
4444	ev_prepare_stop (EV_P_ ev_prepare *w) EV_THROW	5001	ev_prepare_stop (EV_P_ ev_prepare *w) EV_NOEXCEPT
4445	{	5002	{
4446	clear_pending (EV_A_ (W)w);	5003	clear_pending (EV_A_ (W)w);
4447	if (expect_false (!ev_is_active (w)))	5004	if (ecb_expect_false (!ev_is_active (w)))
4448	return;	5005	return;
4449		5006
4450	EV_FREQUENT_CHECK;	5007	EV_FREQUENT_CHECK;
4451		5008
4452	{	5009	{
…		…
4462	}	5019	}
4463	#endif	5020	#endif
4464		5021
4465	#if EV_CHECK_ENABLE	5022	#if EV_CHECK_ENABLE
4466	void	5023	void
4467	ev_check_start (EV_P_ ev_check *w) EV_THROW	5024	ev_check_start (EV_P_ ev_check *w) EV_NOEXCEPT
4468	{	5025	{
4469	if (expect_false (ev_is_active (w)))	5026	if (ecb_expect_false (ev_is_active (w)))
4470	return;	5027	return;
4471		5028
4472	EV_FREQUENT_CHECK;	5029	EV_FREQUENT_CHECK;
4473		5030
4474	ev_start (EV_A_ (W)w, ++checkcnt);	5031	ev_start (EV_A_ (W)w, ++checkcnt);
4475	array_needsize (ev_check *, checks, checkmax, checkcnt, EMPTY2);	5032	array_needsize (ev_check *, checks, checkmax, checkcnt, array_needsize_noinit);
4476	checks [checkcnt - 1] = w;	5033	checks [checkcnt - 1] = w;
4477		5034
4478	EV_FREQUENT_CHECK;	5035	EV_FREQUENT_CHECK;
4479	}	5036	}
4480		5037
4481	void	5038	void
4482	ev_check_stop (EV_P_ ev_check *w) EV_THROW	5039	ev_check_stop (EV_P_ ev_check *w) EV_NOEXCEPT
4483	{	5040	{
4484	clear_pending (EV_A_ (W)w);	5041	clear_pending (EV_A_ (W)w);
4485	if (expect_false (!ev_is_active (w)))	5042	if (ecb_expect_false (!ev_is_active (w)))
4486	return;	5043	return;
4487		5044
4488	EV_FREQUENT_CHECK;	5045	EV_FREQUENT_CHECK;
4489		5046
4490	{	5047	{
…		…
4499	EV_FREQUENT_CHECK;	5056	EV_FREQUENT_CHECK;
4500	}	5057	}
4501	#endif	5058	#endif
4502		5059
4503	#if EV_EMBED_ENABLE	5060	#if EV_EMBED_ENABLE
4504	void noinline	5061	ecb_noinline
		5062	void
4505	ev_embed_sweep (EV_P_ ev_embed *w) EV_THROW	5063	ev_embed_sweep (EV_P_ ev_embed *w) EV_NOEXCEPT
4506	{	5064	{
4507	ev_run (w->other, EVRUN_NOWAIT);	5065	ev_run (w->other, EVRUN_NOWAIT);
4508	}	5066	}
4509		5067
4510	static void	5068	static void
…		…
4532	ev_run (EV_A_ EVRUN_NOWAIT);	5090	ev_run (EV_A_ EVRUN_NOWAIT);
4533	}	5091	}
4534	}	5092	}
4535	}	5093	}
4536		5094
		5095	#if EV_FORK_ENABLE
4537	static void	5096	static void
4538	embed_fork_cb (EV_P_ ev_fork *fork_w, int revents)	5097	embed_fork_cb (EV_P_ ev_fork *fork_w, int revents)
4539	{	5098	{
4540	ev_embed *w = (ev_embed *)(((char *)fork_w) - offsetof (ev_embed, fork));	5099	ev_embed *w = (ev_embed *)(((char *)fork_w) - offsetof (ev_embed, fork));
4541		5100
…		…
4548	ev_run (EV_A_ EVRUN_NOWAIT);	5107	ev_run (EV_A_ EVRUN_NOWAIT);
4549	}	5108	}
4550		5109
4551	ev_embed_start (EV_A_ w);	5110	ev_embed_start (EV_A_ w);
4552	}	5111	}
		5112	#endif
4553		5113
4554	#if 0	5114	#if 0
4555	static void	5115	static void
4556	embed_idle_cb (EV_P_ ev_idle *idle, int revents)	5116	embed_idle_cb (EV_P_ ev_idle *idle, int revents)
4557	{	5117	{
4558	ev_idle_stop (EV_A_ idle);	5118	ev_idle_stop (EV_A_ idle);
4559	}	5119	}
4560	#endif	5120	#endif
4561		5121
4562	void	5122	void
4563	ev_embed_start (EV_P_ ev_embed *w) EV_THROW	5123	ev_embed_start (EV_P_ ev_embed *w) EV_NOEXCEPT
4564	{	5124	{
4565	if (expect_false (ev_is_active (w)))	5125	if (ecb_expect_false (ev_is_active (w)))
4566	return;	5126	return;
4567		5127
4568	{	5128	{
4569	EV_P = w->other;	5129	EV_P = w->other;
4570	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));	5130	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));
…		…
4578		5138
4579	ev_prepare_init (&w->prepare, embed_prepare_cb);	5139	ev_prepare_init (&w->prepare, embed_prepare_cb);
4580	ev_set_priority (&w->prepare, EV_MINPRI);	5140	ev_set_priority (&w->prepare, EV_MINPRI);
4581	ev_prepare_start (EV_A_ &w->prepare);	5141	ev_prepare_start (EV_A_ &w->prepare);
4582		5142
		5143	#if EV_FORK_ENABLE
4583	ev_fork_init (&w->fork, embed_fork_cb);	5144	ev_fork_init (&w->fork, embed_fork_cb);
4584	ev_fork_start (EV_A_ &w->fork);	5145	ev_fork_start (EV_A_ &w->fork);
		5146	#endif
4585		5147
4586	/*ev_idle_init (&w->idle, e,bed_idle_cb);*/	5148	/*ev_idle_init (&w->idle, e,bed_idle_cb);*/
4587		5149
4588	ev_start (EV_A_ (W)w, 1);	5150	ev_start (EV_A_ (W)w, 1);
4589		5151
4590	EV_FREQUENT_CHECK;	5152	EV_FREQUENT_CHECK;
4591	}	5153	}
4592		5154
4593	void	5155	void
4594	ev_embed_stop (EV_P_ ev_embed *w) EV_THROW	5156	ev_embed_stop (EV_P_ ev_embed *w) EV_NOEXCEPT
4595	{	5157	{
4596	clear_pending (EV_A_ (W)w);	5158	clear_pending (EV_A_ (W)w);
4597	if (expect_false (!ev_is_active (w)))	5159	if (ecb_expect_false (!ev_is_active (w)))
4598	return;	5160	return;
4599		5161
4600	EV_FREQUENT_CHECK;	5162	EV_FREQUENT_CHECK;
4601		5163
4602	ev_io_stop (EV_A_ &w->io);	5164	ev_io_stop (EV_A_ &w->io);
4603	ev_prepare_stop (EV_A_ &w->prepare);	5165	ev_prepare_stop (EV_A_ &w->prepare);
		5166	#if EV_FORK_ENABLE
4604	ev_fork_stop (EV_A_ &w->fork);	5167	ev_fork_stop (EV_A_ &w->fork);
		5168	#endif
4605		5169
4606	ev_stop (EV_A_ (W)w);	5170	ev_stop (EV_A_ (W)w);
4607		5171
4608	EV_FREQUENT_CHECK;	5172	EV_FREQUENT_CHECK;
4609	}	5173	}
4610	#endif	5174	#endif
4611		5175
4612	#if EV_FORK_ENABLE	5176	#if EV_FORK_ENABLE
4613	void	5177	void
4614	ev_fork_start (EV_P_ ev_fork *w) EV_THROW	5178	ev_fork_start (EV_P_ ev_fork *w) EV_NOEXCEPT
4615	{	5179	{
4616	if (expect_false (ev_is_active (w)))	5180	if (ecb_expect_false (ev_is_active (w)))
4617	return;	5181	return;
4618		5182
4619	EV_FREQUENT_CHECK;	5183	EV_FREQUENT_CHECK;
4620		5184
4621	ev_start (EV_A_ (W)w, ++forkcnt);	5185	ev_start (EV_A_ (W)w, ++forkcnt);
4622	array_needsize (ev_fork *, forks, forkmax, forkcnt, EMPTY2);	5186	array_needsize (ev_fork *, forks, forkmax, forkcnt, array_needsize_noinit);
4623	forks [forkcnt - 1] = w;	5187	forks [forkcnt - 1] = w;
4624		5188
4625	EV_FREQUENT_CHECK;	5189	EV_FREQUENT_CHECK;
4626	}	5190	}
4627		5191
4628	void	5192	void
4629	ev_fork_stop (EV_P_ ev_fork *w) EV_THROW	5193	ev_fork_stop (EV_P_ ev_fork *w) EV_NOEXCEPT
4630	{	5194	{
4631	clear_pending (EV_A_ (W)w);	5195	clear_pending (EV_A_ (W)w);
4632	if (expect_false (!ev_is_active (w)))	5196	if (ecb_expect_false (!ev_is_active (w)))
4633	return;	5197	return;
4634		5198
4635	EV_FREQUENT_CHECK;	5199	EV_FREQUENT_CHECK;
4636		5200
4637	{	5201	{
…		…
4647	}	5211	}
4648	#endif	5212	#endif
4649		5213
4650	#if EV_CLEANUP_ENABLE	5214	#if EV_CLEANUP_ENABLE
4651	void	5215	void
4652	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_THROW	5216	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4653	{	5217	{
4654	if (expect_false (ev_is_active (w)))	5218	if (ecb_expect_false (ev_is_active (w)))
4655	return;	5219	return;
4656		5220
4657	EV_FREQUENT_CHECK;	5221	EV_FREQUENT_CHECK;
4658		5222
4659	ev_start (EV_A_ (W)w, ++cleanupcnt);	5223	ev_start (EV_A_ (W)w, ++cleanupcnt);
4660	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, EMPTY2);	5224	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, array_needsize_noinit);
4661	cleanups [cleanupcnt - 1] = w;	5225	cleanups [cleanupcnt - 1] = w;
4662		5226
4663	/* cleanup watchers should never keep a refcount on the loop */	5227	/* cleanup watchers should never keep a refcount on the loop */
4664	ev_unref (EV_A);	5228	ev_unref (EV_A);
4665	EV_FREQUENT_CHECK;	5229	EV_FREQUENT_CHECK;
4666	}	5230	}
4667		5231
4668	void	5232	void
4669	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_THROW	5233	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4670	{	5234	{
4671	clear_pending (EV_A_ (W)w);	5235	clear_pending (EV_A_ (W)w);
4672	if (expect_false (!ev_is_active (w)))	5236	if (ecb_expect_false (!ev_is_active (w)))
4673	return;	5237	return;
4674		5238
4675	EV_FREQUENT_CHECK;	5239	EV_FREQUENT_CHECK;
4676	ev_ref (EV_A);	5240	ev_ref (EV_A);
4677		5241
…		…
4688	}	5252	}
4689	#endif	5253	#endif
4690		5254
4691	#if EV_ASYNC_ENABLE	5255	#if EV_ASYNC_ENABLE
4692	void	5256	void
4693	ev_async_start (EV_P_ ev_async *w) EV_THROW	5257	ev_async_start (EV_P_ ev_async *w) EV_NOEXCEPT
4694	{	5258	{
4695	if (expect_false (ev_is_active (w)))	5259	if (ecb_expect_false (ev_is_active (w)))
4696	return;	5260	return;
4697		5261
4698	w->sent = 0;	5262	w->sent = 0;
4699		5263
4700	evpipe_init (EV_A);	5264	evpipe_init (EV_A);
4701		5265
4702	EV_FREQUENT_CHECK;	5266	EV_FREQUENT_CHECK;
4703		5267
4704	ev_start (EV_A_ (W)w, ++asynccnt);	5268	ev_start (EV_A_ (W)w, ++asynccnt);
4705	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, EMPTY2);	5269	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, array_needsize_noinit);
4706	asyncs [asynccnt - 1] = w;	5270	asyncs [asynccnt - 1] = w;
4707		5271
4708	EV_FREQUENT_CHECK;	5272	EV_FREQUENT_CHECK;
4709	}	5273	}
4710		5274
4711	void	5275	void
4712	ev_async_stop (EV_P_ ev_async *w) EV_THROW	5276	ev_async_stop (EV_P_ ev_async *w) EV_NOEXCEPT
4713	{	5277	{
4714	clear_pending (EV_A_ (W)w);	5278	clear_pending (EV_A_ (W)w);
4715	if (expect_false (!ev_is_active (w)))	5279	if (ecb_expect_false (!ev_is_active (w)))
4716	return;	5280	return;
4717		5281
4718	EV_FREQUENT_CHECK;	5282	EV_FREQUENT_CHECK;
4719		5283
4720	{	5284	{
…		…
4728		5292
4729	EV_FREQUENT_CHECK;	5293	EV_FREQUENT_CHECK;
4730	}	5294	}
4731		5295
4732	void	5296	void
4733	ev_async_send (EV_P_ ev_async *w) EV_THROW	5297	ev_async_send (EV_P_ ev_async *w) EV_NOEXCEPT
4734	{	5298	{
4735	w->sent = 1;	5299	w->sent = 1;
4736	evpipe_write (EV_A_ &async_pending);	5300	evpipe_write (EV_A_ &async_pending);
4737	}	5301	}
4738	#endif	5302	#endif
…		…
4775		5339
4776	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));	5340	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));
4777	}	5341	}
4778		5342
4779	void	5343	void
4780	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_THROW	5344	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_NOEXCEPT
4781	{	5345	{
4782	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));	5346	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));
4783
4784	if (expect_false (!once))
4785	{
4786	cb (EV_ERROR | EV_READ | EV_WRITE | EV_TIMER, arg);
4787	return;
4788	}
4789		5347
4790	once->cb = cb;	5348	once->cb = cb;
4791	once->arg = arg;	5349	once->arg = arg;
4792		5350
4793	ev_init (&once->io, once_cb_io);	5351	ev_init (&once->io, once_cb_io);
…		…
4806	}	5364	}
4807		5365
4808	/*****************************************************************************/	5366	/*****************************************************************************/
4809		5367
4810	#if EV_WALK_ENABLE	5368	#if EV_WALK_ENABLE
4811	void ecb_cold	5369	ecb_cold
		5370	void
4812	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_THROW	5371	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_NOEXCEPT
4813	{	5372	{
4814	int i, j;	5373	int i, j;
4815	ev_watcher_list *wl, *wn;	5374	ev_watcher_list *wl, *wn;
4816		5375
4817	if (types & (EV_IO | EV_EMBED))	5376	if (types & (EV_IO | EV_EMBED))

Diff Legend

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