ViewVC Help

View File | Revision Log | Show Annotations | Download File

/cvs/libev/ev.c

Comparing libev/ev.c (file contents):
Revision 1.467 by root, Fri May 16 15:15:39 2014 UTC vs.
Revision 1.515 by root, Fri Dec 20 20:51:46 2019 UTC

1	/*	1	/*
2	* libev event processing core, watcher management	2	* libev event processing core, watcher management
3	*	3	*
4	* Copyright (c) 2007,2008,2009,2010,2011,2012,2013 Marc Alexander Lehmann <libev@schmorp.de>	4	* Copyright (c) 2007-2019 Marc Alexander Lehmann <libev@schmorp.de>
5	* All rights reserved.	5	* All rights reserved.
6	*	6	*
7	* Redistribution and use in source and binary forms, with or without modifica-	7	* Redistribution and use in source and binary forms, with or without modifica-
8	* tion, are permitted provided that the following conditions are met:	8	* tion, are permitted provided that the following conditions are met:
9	*	9	*
…		…
43	# include EV_CONFIG_H	43	# include EV_CONFIG_H
44	# else	44	# else
45	# include "config.h"	45	# include "config.h"
46	# endif	46	# endif
47		47
48	#if HAVE_FLOOR	48	# if HAVE_FLOOR
49	# ifndef EV_USE_FLOOR	49	# ifndef EV_USE_FLOOR
50	# define EV_USE_FLOOR 1	50	# define EV_USE_FLOOR 1
		51	# endif
51	# endif	52	# endif
52	#endif
53		53
54	# if HAVE_CLOCK_SYSCALL	54	# if HAVE_CLOCK_SYSCALL
55	# ifndef EV_USE_CLOCK_SYSCALL	55	# ifndef EV_USE_CLOCK_SYSCALL
56	# define EV_USE_CLOCK_SYSCALL 1	56	# define EV_USE_CLOCK_SYSCALL 1
57	# ifndef EV_USE_REALTIME	57	# ifndef EV_USE_REALTIME
…		…
115	# else	115	# else
116	# undef EV_USE_EPOLL	116	# undef EV_USE_EPOLL
117	# define EV_USE_EPOLL 0	117	# define EV_USE_EPOLL 0
118	# endif	118	# endif
119		119
		120	# if HAVE_LINUX_AIO_ABI_H
		121	# ifndef EV_USE_LINUXAIO
		122	# define EV_USE_LINUXAIO EV_FEATURE_BACKENDS
		123	# endif
		124	# else
		125	# undef EV_USE_LINUXAIO
		126	# define EV_USE_LINUXAIO 0
		127	# endif
		128
		129	# if HAVE_LINUX_FS_H && HAVE_SYS_TIMERFD_H && HAVE_KERNEL_RWF_T
		130	# ifndef EV_USE_IOURING
		131	# define EV_USE_IOURING EV_FEATURE_BACKENDS
		132	# endif
		133	# else
		134	# undef EV_USE_IOURING
		135	# define EV_USE_IOURING 0
		136	# endif
		137
120	# if HAVE_KQUEUE && HAVE_SYS_EVENT_H	138	# if HAVE_KQUEUE && HAVE_SYS_EVENT_H
121	# ifndef EV_USE_KQUEUE	139	# ifndef EV_USE_KQUEUE
122	# define EV_USE_KQUEUE EV_FEATURE_BACKENDS	140	# define EV_USE_KQUEUE EV_FEATURE_BACKENDS
123	# endif	141	# endif
124	# else	142	# else
…		…
159	# endif	177	# endif
160	# else	178	# else
161	# undef EV_USE_EVENTFD	179	# undef EV_USE_EVENTFD
162	# define EV_USE_EVENTFD 0	180	# define EV_USE_EVENTFD 0
163	# endif	181	# endif
164		182
		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
…		…
256	# else	285	# else
257	# define EV_USE_CLOCK_SYSCALL 0	286	# define EV_USE_CLOCK_SYSCALL 0
258	# endif	287	# endif
259	#endif	288	#endif
260		289
		290	#if !(_POSIX_TIMERS > 0)
		291	# ifndef EV_USE_MONOTONIC
		292	# define EV_USE_MONOTONIC 0
		293	# endif
		294	# ifndef EV_USE_REALTIME
		295	# define EV_USE_REALTIME 0
		296	# endif
		297	#endif
		298
261	#ifndef EV_USE_MONOTONIC	299	#ifndef EV_USE_MONOTONIC
262	# if defined _POSIX_MONOTONIC_CLOCK && _POSIX_MONOTONIC_CLOCK >= 0	300	# if defined _POSIX_MONOTONIC_CLOCK && _POSIX_MONOTONIC_CLOCK >= 0
263	# define EV_USE_MONOTONIC EV_FEATURE_OS	301	# define EV_USE_MONOTONIC EV_FEATURE_OS
264	# else	302	# else
265	# define EV_USE_MONOTONIC 0	303	# define EV_USE_MONOTONIC 0
…		…
304		342
305	#ifndef EV_USE_PORT	343	#ifndef EV_USE_PORT
306	# define EV_USE_PORT 0	344	# define EV_USE_PORT 0
307	#endif	345	#endif
308		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 1
		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
309	#ifndef EV_USE_INOTIFY	363	#ifndef EV_USE_INOTIFY
310	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))	364	# if __linux && (__GLIBC__ > 2 || (__GLIBC__ == 2 && __GLIBC_MINOR__ >= 4))
311	# define EV_USE_INOTIFY EV_FEATURE_OS	365	# define EV_USE_INOTIFY EV_FEATURE_OS
312	# else	366	# else
313	# define EV_USE_INOTIFY 0	367	# define EV_USE_INOTIFY 0
…		…
336	# else	390	# else
337	# define EV_USE_SIGNALFD 0	391	# define EV_USE_SIGNALFD 0
338	# endif	392	# endif
339	#endif	393	#endif
340		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
341	#if 0 /* debugging */	403	#if 0 /* debugging */
342	# define EV_VERIFY 3	404	# define EV_VERIFY 3
343	# define EV_USE_4HEAP 1	405	# define EV_USE_4HEAP 1
344	# define EV_HEAP_CACHE_AT 1	406	# define EV_HEAP_CACHE_AT 1
345	#endif	407	#endif
…		…
354		416
355	#ifndef EV_HEAP_CACHE_AT	417	#ifndef EV_HEAP_CACHE_AT
356	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA	418	# define EV_HEAP_CACHE_AT EV_FEATURE_DATA
357	#endif	419	#endif
358		420
359	#ifdef ANDROID	421	#ifdef __ANDROID__
360	/* supposedly, android doesn't typedef fd_mask */	422	/* supposedly, android doesn't typedef fd_mask */
361	# undef EV_USE_SELECT	423	# undef EV_USE_SELECT
362	# define EV_USE_SELECT 0	424	# define EV_USE_SELECT 0
363	/* 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 */
364	# undef EV_USE_CLOCK_SYSCALL	426	# undef EV_USE_CLOCK_SYSCALL
…		…
378	# include <sys/syscall.h>	440	# include <sys/syscall.h>
379	# ifdef SYS_clock_gettime	441	# ifdef SYS_clock_gettime
380	# define clock_gettime(id, ts) syscall (SYS_clock_gettime, (id), (ts))	442	# define clock_gettime(id, ts) syscall (SYS_clock_gettime, (id), (ts))
381	# undef EV_USE_MONOTONIC	443	# undef EV_USE_MONOTONIC
382	# define EV_USE_MONOTONIC 1	444	# define EV_USE_MONOTONIC 1
		445	# define EV_NEED_SYSCALL 1
383	# else	446	# else
384	# undef EV_USE_CLOCK_SYSCALL	447	# undef EV_USE_CLOCK_SYSCALL
385	# define EV_USE_CLOCK_SYSCALL 0	448	# define EV_USE_CLOCK_SYSCALL 0
386	# endif	449	# endif
387	#endif	450	#endif
…		…
401	#if !EV_STAT_ENABLE	464	#if !EV_STAT_ENABLE
402	# undef EV_USE_INOTIFY	465	# undef EV_USE_INOTIFY
403	# define EV_USE_INOTIFY 0	466	# define EV_USE_INOTIFY 0
404	#endif	467	#endif
405		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
406	#if !EV_USE_NANOSLEEP	477	#if !EV_USE_NANOSLEEP
407	/* 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 */
408	# if !defined _WIN32 && !defined __hpux	479	# if !defined _WIN32 && !defined __hpux
409	# 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
410	# endif	506	# endif
411	#endif	507	#endif
412		508
413	#if EV_USE_INOTIFY	509	#if EV_USE_INOTIFY
414	# include <sys/statfs.h>	510	# include <sys/statfs.h>
…		…
419	# define EV_USE_INOTIFY 0	515	# define EV_USE_INOTIFY 0
420	# endif	516	# endif
421	#endif	517	#endif
422		518
423	#if EV_USE_EVENTFD	519	#if EV_USE_EVENTFD
424	/* 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 */
425	# include <stdint.h>	521	# include <stdint.h>
426	# ifndef EFD_NONBLOCK	522	# ifndef EFD_NONBLOCK
427	# define EFD_NONBLOCK O_NONBLOCK	523	# define EFD_NONBLOCK O_NONBLOCK
428	# endif	524	# endif
429	# ifndef EFD_CLOEXEC	525	# ifndef EFD_CLOEXEC
…		…
435	# endif	531	# endif
436	EV_CPP(extern "C") int (eventfd) (unsigned int initval, int flags);	532	EV_CPP(extern "C") int (eventfd) (unsigned int initval, int flags);
437	#endif	533	#endif
438		534
439	#if EV_USE_SIGNALFD	535	#if EV_USE_SIGNALFD
440	/* 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 */
441	# include <stdint.h>	537	# include <stdint.h>
442	# ifndef SFD_NONBLOCK	538	# ifndef SFD_NONBLOCK
443	# define SFD_NONBLOCK O_NONBLOCK	539	# define SFD_NONBLOCK O_NONBLOCK
444	# endif	540	# endif
445	# ifndef SFD_CLOEXEC	541	# ifndef SFD_CLOEXEC
…		…
447	# define SFD_CLOEXEC O_CLOEXEC	543	# define SFD_CLOEXEC O_CLOEXEC
448	# else	544	# else
449	# define SFD_CLOEXEC 02000000	545	# define SFD_CLOEXEC 02000000
450	# endif	546	# endif
451	# endif	547	# endif
452	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);
453		549
454	struct signalfd_siginfo	550	struct signalfd_siginfo
455	{	551	{
456	uint32_t ssi_signo;	552	uint32_t ssi_signo;
457	char pad[128 - sizeof (uint32_t)];	553	char pad[128 - sizeof (uint32_t)];
458	};	554	};
459	#endif	555	#endif
460		556
461	/**/	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	/*****************************************************************************/
462		568
463	#if EV_VERIFY >= 3	569	#if EV_VERIFY >= 3
464	# define EV_FREQUENT_CHECK ev_verify (EV_A)	570	# define EV_FREQUENT_CHECK ev_verify (EV_A)
465	#else	571	#else
466	# define EV_FREQUENT_CHECK do { } while (0)	572	# define EV_FREQUENT_CHECK do { } while (0)
…		…
471	* This value is good at least till the year 4000.	577	* This value is good at least till the year 4000.
472	*/	578	*/
473	#define MIN_INTERVAL 0.0001220703125 /* 1/2**13, good till 4000 */	579	#define MIN_INTERVAL 0.0001220703125 /* 1/2**13, good till 4000 */
474	/*#define MIN_INTERVAL 0.00000095367431640625 /* 1/2**20, good till 2200 */	580	/*#define MIN_INTERVAL 0.00000095367431640625 /* 1/2**20, good till 2200 */
475		581
476	#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) */
477	#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) */
478		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
479	#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)
480	#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
481		602
482	/* 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 */
483	/* ECB.H BEGIN */	604	/* ECB.H BEGIN */
484	/*	605	/*
485	* libecb - http://software.schmorp.de/pkg/libecb	606	* libecb - http://software.schmorp.de/pkg/libecb
486	*	607	*
487	* Copyright (©) 2009-2014 Marc Alexander Lehmann <libecb@schmorp.de>	608	* Copyright (©) 2009-2015 Marc Alexander Lehmann <libecb@schmorp.de>
488	* Copyright (©) 2011 Emanuele Giaquinta	609	* Copyright (©) 2011 Emanuele Giaquinta
489	* All rights reserved.	610	* All rights reserved.
490	*	611	*
491	* Redistribution and use in source and binary forms, with or without modifica-	612	* Redistribution and use in source and binary forms, with or without modifica-
492	* tion, are permitted provided that the following conditions are met:	613	* tion, are permitted provided that the following conditions are met:
…		…
523		644
524	#ifndef ECB_H	645	#ifndef ECB_H
525	#define ECB_H	646	#define ECB_H
526		647
527	/* 16 bits major, 16 bits minor */	648	/* 16 bits major, 16 bits minor */
528	#define ECB_VERSION 0x00010003	649	#define ECB_VERSION 0x00010006
529		650
530	#ifdef _WIN32	651	#ifdef _WIN32
531	typedef signed char int8_t;	652	typedef signed char int8_t;
532	typedef unsigned char uint8_t;	653	typedef unsigned char uint8_t;
533	typedef signed short int16_t;	654	typedef signed short int16_t;
…		…
550	typedef uint32_t uintptr_t;	671	typedef uint32_t uintptr_t;
551	typedef int32_t intptr_t;	672	typedef int32_t intptr_t;
552	#endif	673	#endif
553	#else	674	#else
554	#include <inttypes.h>	675	#include <inttypes.h>
555	#if UINTMAX_MAX > 0xffffffffU	676	#if (defined INTPTR_MAX ? INTPTR_MAX : ULONG_MAX) > 0xffffffffU
556	#define ECB_PTRSIZE 8	677	#define ECB_PTRSIZE 8
557	#else	678	#else
558	#define ECB_PTRSIZE 4	679	#define ECB_PTRSIZE 4
559	#endif	680	#endif
560	#endif	681	#endif
561		682
		683	#define ECB_GCC_AMD64 (__amd64 || __amd64__ || __x86_64 || __x86_64__)
		684	#define ECB_MSVC_AMD64 (_M_AMD64 || _M_X64)
		685
562	/* work around x32 idiocy by defining proper macros */	686	/* work around x32 idiocy by defining proper macros */
563	#if __amd64 || __x86_64 || _M_AMD64 || _M_X64	687	#if ECB_GCC_AMD64 || ECB_MSVC_AMD64
564	#if _ILP32	688	#if _ILP32
565	#define ECB_AMD64_X32 1	689	#define ECB_AMD64_X32 1
566	#else	690	#else
567	#define ECB_AMD64 1	691	#define ECB_AMD64 1
568	#endif	692	#endif
…		…
573	* causing enormous grief in return for some better fake benchmark numbers.	697	* causing enormous grief in return for some better fake benchmark numbers.
574	* or so.	698	* or so.
575	* we try to detect these and simply assume they are not gcc - if they have	699	* we try to detect these and simply assume they are not gcc - if they have
576	* an issue with that they should have done it right in the first place.	700	* an issue with that they should have done it right in the first place.
577	*/	701	*/
578	#ifndef ECB_GCC_VERSION
579	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__	702	#if !defined __GNUC_MINOR__ || defined __INTEL_COMPILER || defined __SUNPRO_C || defined __SUNPRO_CC || defined __llvm__ || defined __clang__
580	#define ECB_GCC_VERSION(major,minor) 0	703	#define ECB_GCC_VERSION(major,minor) 0
581	#else	704	#else
582	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))	705	#define ECB_GCC_VERSION(major,minor) (__GNUC__ > (major) || (__GNUC__ == (major) && __GNUC_MINOR__ >= (minor)))
583	#endif	706	#endif
		707
		708	#define ECB_CLANG_VERSION(major,minor) (__clang_major__ > (major) || (__clang_major__ == (major) && __clang_minor__ >= (minor)))
		709
		710	#if __clang__ && defined __has_builtin
		711	#define ECB_CLANG_BUILTIN(x) __has_builtin (x)
		712	#else
		713	#define ECB_CLANG_BUILTIN(x) 0
		714	#endif
		715
		716	#if __clang__ && defined __has_extension
		717	#define ECB_CLANG_EXTENSION(x) __has_extension (x)
		718	#else
		719	#define ECB_CLANG_EXTENSION(x) 0
584	#endif	720	#endif
585		721
586	#define ECB_CPP (__cplusplus+0)	722	#define ECB_CPP (__cplusplus+0)
587	#define ECB_CPP11 (__cplusplus >= 201103L)	723	#define ECB_CPP11 (__cplusplus >= 201103L)
		724	#define ECB_CPP14 (__cplusplus >= 201402L)
		725	#define ECB_CPP17 (__cplusplus >= 201703L)
588		726
589	#if ECB_CPP	727	#if ECB_CPP
590	#define ECB_C 0	728	#define ECB_C 0
591	#define ECB_STDC_VERSION 0	729	#define ECB_STDC_VERSION 0
592	#else	730	#else
…		…
594	#define ECB_STDC_VERSION __STDC_VERSION__	732	#define ECB_STDC_VERSION __STDC_VERSION__
595	#endif	733	#endif
596		734
597	#define ECB_C99 (ECB_STDC_VERSION >= 199901L)	735	#define ECB_C99 (ECB_STDC_VERSION >= 199901L)
598	#define ECB_C11 (ECB_STDC_VERSION >= 201112L)	736	#define ECB_C11 (ECB_STDC_VERSION >= 201112L)
		737	#define ECB_C17 (ECB_STDC_VERSION >= 201710L)
599		738
600	#if ECB_CPP	739	#if ECB_CPP
601	#define ECB_EXTERN_C extern "C"	740	#define ECB_EXTERN_C extern "C"
602	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {	741	#define ECB_EXTERN_C_BEG ECB_EXTERN_C {
603	#define ECB_EXTERN_C_END }	742	#define ECB_EXTERN_C_END }
…		…
618		757
619	#if ECB_NO_SMP	758	#if ECB_NO_SMP
620	#define ECB_MEMORY_FENCE do { } while (0)	759	#define ECB_MEMORY_FENCE do { } while (0)
621	#endif	760	#endif
622		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
623	#ifndef ECB_MEMORY_FENCE	771	#ifndef ECB_MEMORY_FENCE
624	#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")
625	#if __i386 || __i386__	774	#if __i386 || __i386__
626	#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")
627	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")	776	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
628	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	777	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
629	#elif __amd64 || __amd64__ || __x86_64 || __x86_64__	778	#elif ECB_GCC_AMD64
630	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")	779	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("mfence" : : : "memory")
631	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")	780	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("" : : : "memory")
632	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("")	781	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("" : : : "memory")
633	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__	782	#elif __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__
634	#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 */
635	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \	791	#elif defined __ARM_ARCH_6__ || defined __ARM_ARCH_6J__ \
636	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__	792	|| defined __ARM_ARCH_6K__ || defined __ARM_ARCH_6ZK__ \
		793	|| defined __ARM_ARCH_6T2__
637	#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")
638	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \	795	#elif defined __ARM_ARCH_7__ || defined __ARM_ARCH_7A__ \
639	|| defined __ARM_ARCH_7M__ || defined __ARM_ARCH_7R__	796	|| defined __ARM_ARCH_7R__ || defined __ARM_ARCH_7M__
640	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")	797	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb" : : : "memory")
641	#elif __aarch64__	798	#elif __aarch64__
642	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb ish" : : : "memory")	799	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("dmb ish" : : : "memory")
643	#elif (__sparc || __sparc__) && !__sparcv8	800	#elif (__sparc || __sparc__) && !(__sparc_v8__ || defined __sparcv8)
644	#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")
645	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")	802	#define ECB_MEMORY_FENCE_ACQUIRE __asm__ __volatile__ ("membar #LoadStore | #LoadLoad" : : : "memory")
646	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")	803	#define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore")
647	#elif defined __s390__ || defined __s390x__	804	#elif defined __s390__ || defined __s390x__
648	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")	805	#define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory")
…		…
671	#if ECB_GCC_VERSION(4,7)	828	#if ECB_GCC_VERSION(4,7)
672	/* see comment below (stdatomic.h) about the C11 memory model. */	829	/* see comment below (stdatomic.h) about the C11 memory model. */
673	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)	830	#define ECB_MEMORY_FENCE __atomic_thread_fence (__ATOMIC_SEQ_CST)
674	#define ECB_MEMORY_FENCE_ACQUIRE __atomic_thread_fence (__ATOMIC_ACQUIRE)	831	#define ECB_MEMORY_FENCE_ACQUIRE __atomic_thread_fence (__ATOMIC_ACQUIRE)
675	#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)
676		834
677	/* The __has_feature syntax from clang is so misdesigned that we cannot use it	835	#elif ECB_CLANG_EXTENSION(c_atomic)
678	* without risking compile time errors with other compilers. We *could*
679	* define our own ecb_clang_has_feature, but I just can't be bothered to work
680	* around this shit time and again.
681	* #elif defined __clang && __has_feature (cxx_atomic)
682	* // see comment below (stdatomic.h) about the C11 memory model.	836	/* see comment below (stdatomic.h) about the C11 memory model. */
683	* #define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)	837	#define ECB_MEMORY_FENCE __c11_atomic_thread_fence (__ATOMIC_SEQ_CST)
684	* #define ECB_MEMORY_FENCE_ACQUIRE __c11_atomic_thread_fence (__ATOMIC_ACQUIRE)	838	#define ECB_MEMORY_FENCE_ACQUIRE __c11_atomic_thread_fence (__ATOMIC_ACQUIRE)
685	* #define ECB_MEMORY_FENCE_RELEASE __c11_atomic_thread_fence (__ATOMIC_RELEASE)	839	#define ECB_MEMORY_FENCE_RELEASE __c11_atomic_thread_fence (__ATOMIC_RELEASE)
686	*/	840	#define ECB_MEMORY_FENCE_RELAXED __c11_atomic_thread_fence (__ATOMIC_RELAXED)
687		841
688	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__	842	#elif ECB_GCC_VERSION(4,4) || defined __INTEL_COMPILER || defined __clang__
689	#define ECB_MEMORY_FENCE __sync_synchronize ()	843	#define ECB_MEMORY_FENCE __sync_synchronize ()
690	#elif _MSC_VER >= 1500 /* VC++ 2008 */	844	#elif _MSC_VER >= 1500 /* VC++ 2008 */
691	/* 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... */
…		…
701	#elif defined _WIN32	855	#elif defined _WIN32
702	#include <WinNT.h>	856	#include <WinNT.h>
703	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */	857	#define ECB_MEMORY_FENCE MemoryBarrier () /* actually just xchg on x86... scary */
704	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110	858	#elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110
705	#include <mbarrier.h>	859	#include <mbarrier.h>
706	#define ECB_MEMORY_FENCE __machine_rw_barrier ()	860	#define ECB_MEMORY_FENCE __machine_rw_barrier ()
707	#define ECB_MEMORY_FENCE_ACQUIRE __machine_r_barrier ()	861	#define ECB_MEMORY_FENCE_ACQUIRE __machine_acq_barrier ()
708	#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 ()
709	#elif __xlC__	864	#elif __xlC__
710	#define ECB_MEMORY_FENCE __sync ()	865	#define ECB_MEMORY_FENCE __sync ()
711	#endif	866	#endif
712	#endif	867	#endif
713		868
714	#ifndef ECB_MEMORY_FENCE	869	#ifndef ECB_MEMORY_FENCE
715	#if ECB_C11 && !defined __STDC_NO_ATOMICS__	870	#if ECB_C11 && !defined __STDC_NO_ATOMICS__
716	/* 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, */
717	/* not just C11 atomics and atomic accesses */	872	/* not just C11 atomics and atomic accesses */
718	#include <stdatomic.h>	873	#include <stdatomic.h>
719	/* Unfortunately, neither gcc 4.7 nor clang 3.1 generate any instructions for */
720	/* any fence other than seq_cst, which isn't very efficient for us. */
721	/* Why that is, we don't know - either the C11 memory model is quite useless */
722	/* for most usages, or gcc and clang have a bug */
723	/* I *currently* lean towards the latter, and inefficiently implement */
724	/* all three of ecb's fences as a seq_cst fence */
725	/* Update, gcc-4.8 generates mfence for all c++ fences, but nothing */
726	/* for all __atomic_thread_fence's except seq_cst */
727	#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)
728	#endif	877	#endif
729	#endif	878	#endif
730		879
731	#ifndef ECB_MEMORY_FENCE	880	#ifndef ECB_MEMORY_FENCE
732	#if !ECB_AVOID_PTHREADS	881	#if !ECB_AVOID_PTHREADS
…		…
752		901
753	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE	902	#if !defined ECB_MEMORY_FENCE_RELEASE && defined ECB_MEMORY_FENCE
754	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	903	#define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
755	#endif	904	#endif
756		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
757	/*****************************************************************************/	910	/*****************************************************************************/
758		911
759	#if __cplusplus	912	#if ECB_CPP
760	#define ecb_inline static inline	913	#define ecb_inline static inline
761	#elif ECB_GCC_VERSION(2,5)	914	#elif ECB_GCC_VERSION(2,5)
762	#define ecb_inline static __inline__	915	#define ecb_inline static __inline__
763	#elif ECB_C99	916	#elif ECB_C99
764	#define ecb_inline static inline	917	#define ecb_inline static inline
…		…
778		931
779	#define ECB_CONCAT_(a, b) a ## b	932	#define ECB_CONCAT_(a, b) a ## b
780	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)	933	#define ECB_CONCAT(a, b) ECB_CONCAT_(a, b)
781	#define ECB_STRINGIFY_(a) # a	934	#define ECB_STRINGIFY_(a) # a
782	#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))
783		937
784	#define ecb_function_ ecb_inline	938	#define ecb_function_ ecb_inline
785		939
786	#if ECB_GCC_VERSION(3,1)	940	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_VERSION(2,8)
787	#define ecb_attribute(attrlist) __attribute__(attrlist)	941	#define ecb_attribute(attrlist) __attribute__ (attrlist)
788	#define ecb_is_constant(expr) __builtin_constant_p (expr)
789	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))
790	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)
791	#else	942	#else
792	#define ecb_attribute(attrlist)	943	#define ecb_attribute(attrlist)
		944	#endif
793		945
		946	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_constant_p)
		947	#define ecb_is_constant(expr) __builtin_constant_p (expr)
		948	#else
794	/* possible C11 impl for integral types	949	/* possible C11 impl for integral types
795	typedef struct ecb_is_constant_struct ecb_is_constant_struct;	950	typedef struct ecb_is_constant_struct ecb_is_constant_struct;
796	#define ecb_is_constant(expr) _Generic ((1 ? (struct ecb_is_constant_struct *)0 : (void *)((expr) - (expr)), ecb_is_constant_struct *: 0, default: 1)) */	951	#define ecb_is_constant(expr) _Generic ((1 ? (struct ecb_is_constant_struct *)0 : (void *)((expr) - (expr)), ecb_is_constant_struct *: 0, default: 1)) */
797		952
798	#define ecb_is_constant(expr) 0	953	#define ecb_is_constant(expr) 0
		954	#endif
		955
		956	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_expect)
		957	#define ecb_expect(expr,value) __builtin_expect ((expr),(value))
		958	#else
799	#define ecb_expect(expr,value) (expr)	959	#define ecb_expect(expr,value) (expr)
		960	#endif
		961
		962	#if ECB_GCC_VERSION(3,1) || ECB_CLANG_BUILTIN(__builtin_prefetch)
		963	#define ecb_prefetch(addr,rw,locality) __builtin_prefetch (addr, rw, locality)
		964	#else
800	#define ecb_prefetch(addr,rw,locality)	965	#define ecb_prefetch(addr,rw,locality)
801	#endif	966	#endif
802		967
803	/* no emulation for ecb_decltype */	968	/* no emulation for ecb_decltype */
804	#if ECB_GCC_VERSION(4,5)	969	#if ECB_CPP11
		970	// older implementations might have problems with decltype(x)::type, work around it
		971	template<class T> struct ecb_decltype_t { typedef T type; };
805	#define ecb_decltype(x) __decltype(x)	972	#define ecb_decltype(x) ecb_decltype_t<decltype (x)>::type
806	#elif ECB_GCC_VERSION(3,0)	973	#elif ECB_GCC_VERSION(3,0) || ECB_CLANG_VERSION(2,8)
807	#define ecb_decltype(x) __typeof(x)	974	#define ecb_decltype(x) __typeof__ (x)
808	#endif	975	#endif
809		976
		977	#if _MSC_VER >= 1300
		978	#define ecb_deprecated __declspec (deprecated)
		979	#else
		980	#define ecb_deprecated ecb_attribute ((__deprecated__))
		981	#endif
		982
		983	#if _MSC_VER >= 1500
		984	#define ecb_deprecated_message(msg) __declspec (deprecated (msg))
		985	#elif ECB_GCC_VERSION(4,5)
		986	#define ecb_deprecated_message(msg) ecb_attribute ((__deprecated__ (msg))
		987	#else
		988	#define ecb_deprecated_message(msg) ecb_deprecated
		989	#endif
		990
		991	#if _MSC_VER >= 1400
		992	#define ecb_noinline __declspec (noinline)
		993	#else
810	#define ecb_noinline ecb_attribute ((__noinline__))	994	#define ecb_noinline ecb_attribute ((__noinline__))
		995	#endif
		996
811	#define ecb_unused ecb_attribute ((__unused__))	997	#define ecb_unused ecb_attribute ((__unused__))
812	#define ecb_const ecb_attribute ((__const__))	998	#define ecb_const ecb_attribute ((__const__))
813	#define ecb_pure ecb_attribute ((__pure__))	999	#define ecb_pure ecb_attribute ((__pure__))
814		1000
815	#if ECB_C11	1001	#if ECB_C11 || __IBMC_NORETURN
		1002	/* http://www-01.ibm.com/support/knowledgecenter/SSGH3R_13.1.0/com.ibm.xlcpp131.aix.doc/language_ref/noreturn.html */
816	#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)
817	#else	1009	#else
818	#define ecb_noreturn ecb_attribute ((__noreturn__))	1010	#define ecb_noreturn ecb_attribute ((__noreturn__))
819	#endif	1011	#endif
820		1012
821	#if ECB_GCC_VERSION(4,3)	1013	#if ECB_GCC_VERSION(4,3)
…		…
836	/* for compatibility to the rest of the world */	1028	/* for compatibility to the rest of the world */
837	#define ecb_likely(expr) ecb_expect_true (expr)	1029	#define ecb_likely(expr) ecb_expect_true (expr)
838	#define ecb_unlikely(expr) ecb_expect_false (expr)	1030	#define ecb_unlikely(expr) ecb_expect_false (expr)
839		1031
840	/* count trailing zero bits and count # of one bits */	1032	/* count trailing zero bits and count # of one bits */
841	#if ECB_GCC_VERSION(3,4)	1033	#if ECB_GCC_VERSION(3,4) \
		1034	|| (ECB_CLANG_BUILTIN(__builtin_clz) && ECB_CLANG_BUILTIN(__builtin_clzll) \
		1035	&& ECB_CLANG_BUILTIN(__builtin_ctz) && ECB_CLANG_BUILTIN(__builtin_ctzll) \
		1036	&& ECB_CLANG_BUILTIN(__builtin_popcount))
842	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */	1037	/* we assume int == 32 bit, long == 32 or 64 bit and long long == 64 bit */
843	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)	1038	#define ecb_ld32(x) (__builtin_clz (x) ^ 31)
844	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)	1039	#define ecb_ld64(x) (__builtin_clzll (x) ^ 63)
845	#define ecb_ctz32(x) __builtin_ctz (x)	1040	#define ecb_ctz32(x) __builtin_ctz (x)
846	#define ecb_ctz64(x) __builtin_ctzll (x)	1041	#define ecb_ctz64(x) __builtin_ctzll (x)
847	#define ecb_popcount32(x) __builtin_popcount (x)	1042	#define ecb_popcount32(x) __builtin_popcount (x)
848	/* no popcountll */	1043	/* no popcountll */
849	#else	1044	#else
850	ecb_function_ int ecb_ctz32 (uint32_t x) ecb_const;	1045	ecb_function_ ecb_const int ecb_ctz32 (uint32_t x);
851	ecb_function_ int	1046	ecb_function_ ecb_const int
852	ecb_ctz32 (uint32_t x)	1047	ecb_ctz32 (uint32_t x)
853	{	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
854	int r = 0;	1054	int r = 0;
855		1055
856	x &= ~x + 1; /* this isolates the lowest bit */	1056	x &= ~x + 1; /* this isolates the lowest bit */
857		1057
858	#if ECB_branchless_on_i386	1058	#if ECB_branchless_on_i386
…		…
868	if (x & 0xff00ff00) r += 8;	1068	if (x & 0xff00ff00) r += 8;
869	if (x & 0xffff0000) r += 16;	1069	if (x & 0xffff0000) r += 16;
870	#endif	1070	#endif
871		1071
872	return r;	1072	return r;
		1073	#endif
873	}	1074	}
874		1075
875	ecb_function_ int ecb_ctz64 (uint64_t x) ecb_const;	1076	ecb_function_ ecb_const int ecb_ctz64 (uint64_t x);
876	ecb_function_ int	1077	ecb_function_ ecb_const int
877	ecb_ctz64 (uint64_t x)	1078	ecb_ctz64 (uint64_t x)
878	{	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
879	int shift = x & 0xffffffffU ? 0 : 32;	1085	int shift = x & 0xffffffff ? 0 : 32;
880	return ecb_ctz32 (x >> shift) + shift;	1086	return ecb_ctz32 (x >> shift) + shift;
		1087	#endif
881	}	1088	}
882		1089
883	ecb_function_ int ecb_popcount32 (uint32_t x) ecb_const;	1090	ecb_function_ ecb_const int ecb_popcount32 (uint32_t x);
884	ecb_function_ int	1091	ecb_function_ ecb_const int
885	ecb_popcount32 (uint32_t x)	1092	ecb_popcount32 (uint32_t x)
886	{	1093	{
887	x -= (x >> 1) & 0x55555555;	1094	x -= (x >> 1) & 0x55555555;
888	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);	1095	x = ((x >> 2) & 0x33333333) + (x & 0x33333333);
889	x = ((x >> 4) + x) & 0x0f0f0f0f;	1096	x = ((x >> 4) + x) & 0x0f0f0f0f;
890	x *= 0x01010101;	1097	x *= 0x01010101;
891		1098
892	return x >> 24;	1099	return x >> 24;
893	}	1100	}
894		1101
895	ecb_function_ int ecb_ld32 (uint32_t x) ecb_const;	1102	ecb_function_ ecb_const int ecb_ld32 (uint32_t x);
896	ecb_function_ int ecb_ld32 (uint32_t x)	1103	ecb_function_ ecb_const int ecb_ld32 (uint32_t x)
897	{	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
898	int r = 0;	1110	int r = 0;
899		1111
900	if (x >> 16) { x >>= 16; r += 16; }	1112	if (x >> 16) { x >>= 16; r += 16; }
901	if (x >> 8) { x >>= 8; r += 8; }	1113	if (x >> 8) { x >>= 8; r += 8; }
902	if (x >> 4) { x >>= 4; r += 4; }	1114	if (x >> 4) { x >>= 4; r += 4; }
903	if (x >> 2) { x >>= 2; r += 2; }	1115	if (x >> 2) { x >>= 2; r += 2; }
904	if (x >> 1) { r += 1; }	1116	if (x >> 1) { r += 1; }
905		1117
906	return r;	1118	return r;
		1119	#endif
907	}	1120	}
908		1121
909	ecb_function_ int ecb_ld64 (uint64_t x) ecb_const;	1122	ecb_function_ ecb_const int ecb_ld64 (uint64_t x);
910	ecb_function_ int ecb_ld64 (uint64_t x)	1123	ecb_function_ ecb_const int ecb_ld64 (uint64_t x)
911	{	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
912	int r = 0;	1130	int r = 0;
913		1131
914	if (x >> 32) { x >>= 32; r += 32; }	1132	if (x >> 32) { x >>= 32; r += 32; }
915		1133
916	return r + ecb_ld32 (x);	1134	return r + ecb_ld32 (x);
		1135	#endif
917	}	1136	}
918	#endif	1137	#endif
919		1138
920	ecb_function_ ecb_bool ecb_is_pot32 (uint32_t x) ecb_const;	1139	ecb_function_ ecb_const ecb_bool ecb_is_pot32 (uint32_t x);
921	ecb_function_ 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)); }
922	ecb_function_ ecb_bool ecb_is_pot64 (uint64_t x) ecb_const;	1141	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x);
923	ecb_function_ ecb_bool ecb_is_pot64 (uint64_t x) { return !(x & (x - 1)); }	1142	ecb_function_ ecb_const ecb_bool ecb_is_pot64 (uint64_t x) { return !(x & (x - 1)); }
924		1143
925	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x) ecb_const;	1144	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x);
926	ecb_function_ uint8_t ecb_bitrev8 (uint8_t x)	1145	ecb_function_ ecb_const uint8_t ecb_bitrev8 (uint8_t x)
927	{	1146	{
928	return ( (x * 0x0802U & 0x22110U)	1147	return ( (x * 0x0802U & 0x22110U)
929	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;	1148	| (x * 0x8020U & 0x88440U)) * 0x10101U >> 16;
930	}	1149	}
931		1150
932	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x) ecb_const;	1151	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x);
933	ecb_function_ uint16_t ecb_bitrev16 (uint16_t x)	1152	ecb_function_ ecb_const uint16_t ecb_bitrev16 (uint16_t x)
934	{	1153	{
935	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);	1154	x = ((x >> 1) & 0x5555) | ((x & 0x5555) << 1);
936	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);	1155	x = ((x >> 2) & 0x3333) | ((x & 0x3333) << 2);
937	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);	1156	x = ((x >> 4) & 0x0f0f) | ((x & 0x0f0f) << 4);
938	x = ( x >> 8 ) | ( x << 8);	1157	x = ( x >> 8 ) | ( x << 8);
939		1158
940	return x;	1159	return x;
941	}	1160	}
942		1161
943	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x) ecb_const;	1162	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x);
944	ecb_function_ uint32_t ecb_bitrev32 (uint32_t x)	1163	ecb_function_ ecb_const uint32_t ecb_bitrev32 (uint32_t x)
945	{	1164	{
946	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);	1165	x = ((x >> 1) & 0x55555555) | ((x & 0x55555555) << 1);
947	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);	1166	x = ((x >> 2) & 0x33333333) | ((x & 0x33333333) << 2);
948	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);	1167	x = ((x >> 4) & 0x0f0f0f0f) | ((x & 0x0f0f0f0f) << 4);
949	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);	1168	x = ((x >> 8) & 0x00ff00ff) | ((x & 0x00ff00ff) << 8);
…		…
952	return x;	1171	return x;
953	}	1172	}
954		1173
955	/* popcount64 is only available on 64 bit cpus as gcc builtin */	1174	/* popcount64 is only available on 64 bit cpus as gcc builtin */
956	/* so for this version we are lazy */	1175	/* so for this version we are lazy */
957	ecb_function_ int ecb_popcount64 (uint64_t x) ecb_const;	1176	ecb_function_ ecb_const int ecb_popcount64 (uint64_t x);
958	ecb_function_ int	1177	ecb_function_ ecb_const int
959	ecb_popcount64 (uint64_t x)	1178	ecb_popcount64 (uint64_t x)
960	{	1179	{
961	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);	1180	return ecb_popcount32 (x) + ecb_popcount32 (x >> 32);
962	}	1181	}
963		1182
964	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) ecb_const;	1183	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count);
965	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) ecb_const;	1184	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count);
966	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) ecb_const;	1185	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count);
967	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) ecb_const;	1186	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count);
968	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) ecb_const;	1187	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count);
969	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) ecb_const;	1188	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count);
970	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) ecb_const;	1189	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count);
971	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) ecb_const;	1190	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count);
972		1191
973	ecb_inline uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }	1192	ecb_inline ecb_const uint8_t ecb_rotl8 (uint8_t x, unsigned int count) { return (x >> ( 8 - count)) | (x << count); }
974	ecb_inline uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }	1193	ecb_inline ecb_const uint8_t ecb_rotr8 (uint8_t x, unsigned int count) { return (x << ( 8 - count)) | (x >> count); }
975	ecb_inline uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }	1194	ecb_inline ecb_const uint16_t ecb_rotl16 (uint16_t x, unsigned int count) { return (x >> (16 - count)) | (x << count); }
976	ecb_inline uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }	1195	ecb_inline ecb_const uint16_t ecb_rotr16 (uint16_t x, unsigned int count) { return (x << (16 - count)) | (x >> count); }
977	ecb_inline uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }	1196	ecb_inline ecb_const uint32_t ecb_rotl32 (uint32_t x, unsigned int count) { return (x >> (32 - count)) | (x << count); }
978	ecb_inline uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }	1197	ecb_inline ecb_const uint32_t ecb_rotr32 (uint32_t x, unsigned int count) { return (x << (32 - count)) | (x >> count); }
979	ecb_inline uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }	1198	ecb_inline ecb_const uint64_t ecb_rotl64 (uint64_t x, unsigned int count) { return (x >> (64 - count)) | (x << count); }
980	ecb_inline uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }	1199	ecb_inline ecb_const uint64_t ecb_rotr64 (uint64_t x, unsigned int count) { return (x << (64 - count)) | (x >> count); }
981		1200
982	#if ECB_GCC_VERSION(4,3)	1201	#if ECB_GCC_VERSION(4,3) || (ECB_CLANG_BUILTIN(__builtin_bswap32) && ECB_CLANG_BUILTIN(__builtin_bswap64))
		1202	#if ECB_GCC_VERSION(4,8) || ECB_CLANG_BUILTIN(__builtin_bswap16)
		1203	#define ecb_bswap16(x) __builtin_bswap16 (x)
		1204	#else
983	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)	1205	#define ecb_bswap16(x) (__builtin_bswap32 (x) >> 16)
		1206	#endif
984	#define ecb_bswap32(x) __builtin_bswap32 (x)	1207	#define ecb_bswap32(x) __builtin_bswap32 (x)
985	#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)))
986	#else	1214	#else
987	ecb_function_ uint16_t ecb_bswap16 (uint16_t x) ecb_const;	1215	ecb_function_ ecb_const uint16_t ecb_bswap16 (uint16_t x);
988	ecb_function_ uint16_t	1216	ecb_function_ ecb_const uint16_t
989	ecb_bswap16 (uint16_t x)	1217	ecb_bswap16 (uint16_t x)
990	{	1218	{
991	return ecb_rotl16 (x, 8);	1219	return ecb_rotl16 (x, 8);
992	}	1220	}
993		1221
994	ecb_function_ uint32_t ecb_bswap32 (uint32_t x) ecb_const;	1222	ecb_function_ ecb_const uint32_t ecb_bswap32 (uint32_t x);
995	ecb_function_ uint32_t	1223	ecb_function_ ecb_const uint32_t
996	ecb_bswap32 (uint32_t x)	1224	ecb_bswap32 (uint32_t x)
997	{	1225	{
998	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);	1226	return (((uint32_t)ecb_bswap16 (x)) << 16) | ecb_bswap16 (x >> 16);
999	}	1227	}
1000		1228
1001	ecb_function_ uint64_t ecb_bswap64 (uint64_t x) ecb_const;	1229	ecb_function_ ecb_const uint64_t ecb_bswap64 (uint64_t x);
1002	ecb_function_ uint64_t	1230	ecb_function_ ecb_const uint64_t
1003	ecb_bswap64 (uint64_t x)	1231	ecb_bswap64 (uint64_t x)
1004	{	1232	{
1005	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);	1233	return (((uint64_t)ecb_bswap32 (x)) << 32) | ecb_bswap32 (x >> 32);
1006	}	1234	}
1007	#endif	1235	#endif
1008		1236
1009	#if ECB_GCC_VERSION(4,5)	1237	#if ECB_GCC_VERSION(4,5) || ECB_CLANG_BUILTIN(__builtin_unreachable)
1010	#define ecb_unreachable() __builtin_unreachable ()	1238	#define ecb_unreachable() __builtin_unreachable ()
1011	#else	1239	#else
1012	/* this seems to work fine, but gcc always emits a warning for it :/ */	1240	/* this seems to work fine, but gcc always emits a warning for it :/ */
1013	ecb_inline void ecb_unreachable (void) ecb_noreturn;	1241	ecb_inline ecb_noreturn void ecb_unreachable (void);
1014	ecb_inline void ecb_unreachable (void) { }	1242	ecb_inline ecb_noreturn void ecb_unreachable (void) { }
1015	#endif	1243	#endif
1016		1244
1017	/* try to tell the compiler that some condition is definitely true */	1245	/* try to tell the compiler that some condition is definitely true */
1018	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0	1246	#define ecb_assume(cond) if (!(cond)) ecb_unreachable (); else 0
1019		1247
1020	ecb_inline unsigned char ecb_byteorder_helper (void) ecb_const;	1248	ecb_inline ecb_const uint32_t ecb_byteorder_helper (void);
1021	ecb_inline unsigned char	1249	ecb_inline ecb_const uint32_t
1022	ecb_byteorder_helper (void)	1250	ecb_byteorder_helper (void)
1023	{	1251	{
1024	/* the union code still generates code under pressure in gcc, */	1252	/* the union code still generates code under pressure in gcc, */
1025	/* but less than using pointers, and always seems to */	1253	/* but less than using pointers, and always seems to */
1026	/* successfully return a constant. */	1254	/* successfully return a constant. */
1027	/* the reason why we have this horrible preprocessor mess */	1255	/* the reason why we have this horrible preprocessor mess */
1028	/* 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 */
1029	/* or when using a recent enough gcc version (>= 4.6) */	1257	/* or when using a recent enough gcc version (>= 4.6) */
1030	#if __i386 || __i386__ || _M_X86 || __amd64 || __amd64__ || _M_X64
1031	return 0x44;
1032	#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
1033	return 0x44;	1261	return 0x44332211;
1034	#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
1035	return 0x11;	1265	return 0x11223344;
1036	#else	1266	#else
1037	union	1267	union
1038	{	1268	{
		1269	uint8_t c[4];
1039	uint32_t i;	1270	uint32_t u;
1040	uint8_t c;
1041	} u = { 0x11223344 };	1271	} u = { 0x11, 0x22, 0x33, 0x44 };
1042	return u.c;	1272	return u.u;
1043	#endif	1273	#endif
1044	}	1274	}
1045		1275
1046	ecb_inline ecb_bool ecb_big_endian (void) ecb_const;	1276	ecb_inline ecb_const ecb_bool ecb_big_endian (void);
1047	ecb_inline ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11; }	1277	ecb_inline ecb_const ecb_bool ecb_big_endian (void) { return ecb_byteorder_helper () == 0x11223344; }
1048	ecb_inline ecb_bool ecb_little_endian (void) ecb_const;	1278	ecb_inline ecb_const ecb_bool ecb_little_endian (void);
1049	ecb_inline ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44; }	1279	ecb_inline ecb_const ecb_bool ecb_little_endian (void) { return ecb_byteorder_helper () == 0x44332211; }
1050		1280
1051	#if ECB_GCC_VERSION(3,0) || ECB_C99	1281	#if ECB_GCC_VERSION(3,0) || ECB_C99
1052	#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))
1053	#else	1283	#else
1054	#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)))
1055	#endif	1285	#endif
1056		1286
1057	#if __cplusplus	1287	#if ECB_CPP
1058	template<typename T>	1288	template<typename T>
1059	static inline T ecb_div_rd (T val, T div)	1289	static inline T ecb_div_rd (T val, T div)
1060	{	1290	{
1061	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;	1291	return val < 0 ? - ((-val + div - 1) / div) : (val ) / div;
1062	}	1292	}
…		…
1079	}	1309	}
1080	#else	1310	#else
1081	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))	1311	#define ecb_array_length(name) (sizeof (name) / sizeof (name [0]))
1082	#endif	1312	#endif
1083		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
1084	/*******************************************************************************/	1410	/*******************************************************************************/
1085	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */	1411	/* floating point stuff, can be disabled by defining ECB_NO_LIBM */
1086		1412
1087	/* basically, everything uses "ieee pure-endian" floating point numbers */	1413	/* basically, everything uses "ieee pure-endian" floating point numbers */
1088	/* the only noteworthy exception is ancient armle, which uses order 43218765 */	1414	/* the only noteworthy exception is ancient armle, which uses order 43218765 */
1089	#if 0 \	1415	#if 0 \
1090	|| __i386 || __i386__ \	1416	|| __i386 || __i386__ \
1091	|| __amd64 || __amd64__ || __x86_64 || __x86_64__ \	1417	|| ECB_GCC_AMD64 \
1092	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \	1418	|| __powerpc__ || __ppc__ || __powerpc64__ || __ppc64__ \
1093	|| defined __s390__ || defined __s390x__ \	1419	|| defined __s390__ || defined __s390x__ \
1094	|| defined __mips__ \	1420	|| defined __mips__ \
1095	|| defined __alpha__ \	1421	|| defined __alpha__ \
1096	|| defined __hppa__ \	1422	|| defined __hppa__ \
1097	|| defined __ia64__ \	1423	|| defined __ia64__ \
1098	|| defined __m68k__ \	1424	|| defined __m68k__ \
1099	|| defined __m88k__ \	1425	|| defined __m88k__ \
1100	|| defined __sh__ \	1426	|| defined __sh__ \
1101	|| defined _M_IX86 || defined _M_AMD64 || defined _M_IA64 \	1427	|| defined _M_IX86 || defined ECB_MSVC_AMD64 || defined _M_IA64 \
1102	|| (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__)) \
1103	|| defined __aarch64__	1429	|| defined __aarch64__
1104	#define ECB_STDFP 1	1430	#define ECB_STDFP 1
1105	#include <string.h> /* for memcpy */	1431	#include <string.h> /* for memcpy */
1106	#else	1432	#else
…		…
1122	#define ECB_NAN NAN	1448	#define ECB_NAN NAN
1123	#else	1449	#else
1124	#define ECB_NAN ECB_INFINITY	1450	#define ECB_NAN ECB_INFINITY
1125	#endif	1451	#endif
1126		1452
1127	/* converts an ieee half/binary16 to a float */	1453	#if ECB_C99 || _XOPEN_VERSION >= 600 || _POSIX_VERSION >= 200112L
1128	ecb_function_ float ecb_binary16_to_float (uint16_t x) ecb_const;	1454	#define ecb_ldexpf(x,e) ldexpf ((x), (e))
1129	ecb_function_ float	1455	#define ecb_frexpf(x,e) frexpf ((x), (e))
1130	ecb_binary16_to_float (uint16_t x)	1456	#else
1131	{	1457	#define ecb_ldexpf(x,e) (float) ldexp ((double) (x), (e))
1132	int e = (x >> 10) & 0x1f;	1458	#define ecb_frexpf(x,e) (float) frexp ((double) (x), (e))
1133	int m = x & 0x3ff;	1459	#endif
1134	float r;
1135
1136	if (!e ) r = ldexpf (m , -24);
1137	else if (e != 31) r = ldexpf (m + 0x400, e - 25);
1138	else if (m ) r = ECB_NAN;
1139	else r = ECB_INFINITY;
1140
1141	return x & 0x8000 ? -r : r;
1142	}
1143		1460
1144	/* convert a float to ieee single/binary32 */	1461	/* convert a float to ieee single/binary32 */
1145	ecb_function_ uint32_t ecb_float_to_binary32 (float x) ecb_const;	1462	ecb_function_ ecb_const uint32_t ecb_float_to_binary32 (float x);
1146	ecb_function_ uint32_t	1463	ecb_function_ ecb_const uint32_t
1147	ecb_float_to_binary32 (float x)	1464	ecb_float_to_binary32 (float x)
1148	{	1465	{
1149	uint32_t r;	1466	uint32_t r;
1150		1467
1151	#if ECB_STDFP	1468	#if ECB_STDFP
…		…
1158	if (x == 0e0f ) return 0x00000000U;	1475	if (x == 0e0f ) return 0x00000000U;
1159	if (x > +3.40282346638528860e+38f) return 0x7f800000U;	1476	if (x > +3.40282346638528860e+38f) return 0x7f800000U;
1160	if (x < -3.40282346638528860e+38f) return 0xff800000U;	1477	if (x < -3.40282346638528860e+38f) return 0xff800000U;
1161	if (x != x ) return 0x7fbfffffU;	1478	if (x != x ) return 0x7fbfffffU;
1162		1479
1163	m = frexpf (x, &e) * 0x1000000U;	1480	m = ecb_frexpf (x, &e) * 0x1000000U;
1164		1481
1165	r = m & 0x80000000U;	1482	r = m & 0x80000000U;
1166		1483
1167	if (r)	1484	if (r)
1168	m = -m;	1485	m = -m;
…		…
1180		1497
1181	return r;	1498	return r;
1182	}	1499	}
1183		1500
1184	/* converts an ieee single/binary32 to a float */	1501	/* converts an ieee single/binary32 to a float */
1185	ecb_function_ float ecb_binary32_to_float (uint32_t x) ecb_const;	1502	ecb_function_ ecb_const float ecb_binary32_to_float (uint32_t x);
1186	ecb_function_ float	1503	ecb_function_ ecb_const float
1187	ecb_binary32_to_float (uint32_t x)	1504	ecb_binary32_to_float (uint32_t x)
1188	{	1505	{
1189	float r;	1506	float r;
1190		1507
1191	#if ECB_STDFP	1508	#if ECB_STDFP
…		…
1201	x |= 0x800000U;	1518	x |= 0x800000U;
1202	else	1519	else
1203	e = 1;	1520	e = 1;
1204		1521
1205	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */	1522	/* we distrust ldexpf a bit and do the 2**-24 scaling by an extra multiply */
1206	r = ldexpf (x * (0.5f / 0x800000U), e - 126);	1523	r = ecb_ldexpf (x * (0.5f / 0x800000U), e - 126);
1207		1524
1208	r = neg ? -r : r;	1525	r = neg ? -r : r;
1209	#endif	1526	#endif
1210		1527
1211	return r;	1528	return r;
1212	}	1529	}
1213		1530
1214	/* convert a double to ieee double/binary64 */	1531	/* convert a double to ieee double/binary64 */
1215	ecb_function_ uint64_t ecb_double_to_binary64 (double x) ecb_const;	1532	ecb_function_ ecb_const uint64_t ecb_double_to_binary64 (double x);
1216	ecb_function_ uint64_t	1533	ecb_function_ ecb_const uint64_t
1217	ecb_double_to_binary64 (double x)	1534	ecb_double_to_binary64 (double x)
1218	{	1535	{
1219	uint64_t r;	1536	uint64_t r;
1220		1537
1221	#if ECB_STDFP	1538	#if ECB_STDFP
…		…
1250		1567
1251	return r;	1568	return r;
1252	}	1569	}
1253		1570
1254	/* converts an ieee double/binary64 to a double */	1571	/* converts an ieee double/binary64 to a double */
1255	ecb_function_ double ecb_binary64_to_double (uint64_t x) ecb_const;	1572	ecb_function_ ecb_const double ecb_binary64_to_double (uint64_t x);
1256	ecb_function_ double	1573	ecb_function_ ecb_const double
1257	ecb_binary64_to_double (uint64_t x)	1574	ecb_binary64_to_double (uint64_t x)
1258	{	1575	{
1259	double r;	1576	double r;
1260		1577
1261	#if ECB_STDFP	1578	#if ECB_STDFP
…		…
1279	#endif	1596	#endif
1280		1597
1281	return r;	1598	return r;
1282	}	1599	}
1283		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
1284	#endif	1617	#endif
1285		1618
1286	#endif	1619	#endif
1287		1620
1288	/* ECB.H END */	1621	/* ECB.H END */
1289		1622
1290	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS	1623	#if ECB_MEMORY_FENCE_NEEDS_PTHREADS
1291	/* 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
1292	* 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
1293	* 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
1294	* libev, in which cases the memory fences become nops.	1627	* libev, in which cases the memory fences become nops.
1295	* alternatively, you can remove this #error and link against libpthread,	1628	* alternatively, you can remove this #error and link against libpthread,
1296	* which will then provide the memory fences.	1629	* which will then provide the memory fences.
1297	*/	1630	*/
1298	# error "memory fences not defined for your architecture, please report"	1631	# error "memory fences not defined for your architecture, please report"
…		…
1302	# define ECB_MEMORY_FENCE do { } while (0)	1635	# define ECB_MEMORY_FENCE do { } while (0)
1303	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE	1636	# define ECB_MEMORY_FENCE_ACQUIRE ECB_MEMORY_FENCE
1304	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE	1637	# define ECB_MEMORY_FENCE_RELEASE ECB_MEMORY_FENCE
1305	#endif	1638	#endif
1306		1639
1307	#define expect_false(cond) ecb_expect_false (cond)
1308	#define expect_true(cond) ecb_expect_true (cond)
1309	#define noinline ecb_noinline
1310
1311	#define inline_size ecb_inline	1640	#define inline_size ecb_inline
1312		1641
1313	#if EV_FEATURE_CODE	1642	#if EV_FEATURE_CODE
1314	# define inline_speed ecb_inline	1643	# define inline_speed ecb_inline
1315	#else	1644	#else
1316	# define inline_speed static noinline	1645	# define inline_speed ecb_noinline static
1317	#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 && !defined __OPTIMIZE_SIZE__
		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	/*****************************************************************************/
1318		1713
1319	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)	1714	#define NUMPRI (EV_MAXPRI - EV_MINPRI + 1)
1320		1715
1321	#if EV_MINPRI == EV_MAXPRI	1716	#if EV_MINPRI == EV_MAXPRI
1322	# define ABSPRI(w) (((W)w), 0)	1717	# define ABSPRI(w) (((W)w), 0)
1323	#else	1718	#else
1324	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)	1719	# define ABSPRI(w) (((W)w)->priority - EV_MINPRI)
1325	#endif	1720	#endif
1326		1721
1327	#define EMPTY /* required for microsofts broken pseudo-c compiler */	1722	#define EMPTY /* required for microsofts broken pseudo-c compiler */
1328	#define EMPTY2(a,b) /* used to suppress some warnings */
1329		1723
1330	typedef ev_watcher *W;	1724	typedef ev_watcher *W;
1331	typedef ev_watcher_list *WL;	1725	typedef ev_watcher_list *WL;
1332	typedef ev_watcher_time *WT;	1726	typedef ev_watcher_time *WT;
1333		1727
…		…
1358	# include "ev_win32.c"	1752	# include "ev_win32.c"
1359	#endif	1753	#endif
1360		1754
1361	/*****************************************************************************/	1755	/*****************************************************************************/
1362		1756
		1757	#if EV_USE_LINUXAIO
		1758	# include <linux/aio_abi.h> /* probably only needed for aio_context_t */
		1759	#endif
		1760
1363	/* define a suitable floor function (only used by periodics atm) */	1761	/* define a suitable floor function (only used by periodics atm) */
1364		1762
1365	#if EV_USE_FLOOR	1763	#if EV_USE_FLOOR
1366	# include <math.h>	1764	# include <math.h>
1367	# define ev_floor(v) floor (v)	1765	# define ev_floor(v) floor (v)
1368	#else	1766	#else
1369		1767
1370	#include <float.h>	1768	#include <float.h>
1371		1769
1372	/* 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
1373	static ev_tstamp noinline	1772	static ev_tstamp
1374	ev_floor (ev_tstamp v)	1773	ev_floor (ev_tstamp v)
1375	{	1774	{
1376	/* the choice of shift factor is not terribly important */	1775	/* the choice of shift factor is not terribly important */
1377	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */	1776	#if FLT_RADIX != 2 /* assume FLT_RADIX == 10 */
1378	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;	1777	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 10000000000000000000. : 1000000000.;
1379	#else	1778	#else
1380	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;	1779	const ev_tstamp shift = sizeof (unsigned long) >= 8 ? 18446744073709551616. : 4294967296.;
1381	#endif	1780	#endif
1382		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
1383	/* argument too large for an unsigned long? */	1790	/* argument too large for an unsigned long? then reduce it */
1384	if (expect_false (v >= shift))	1791	if (ecb_expect_false (v >= shift))
1385	{	1792	{
1386	ev_tstamp f;	1793	ev_tstamp f;
1387		1794
1388	if (v == v - 1.)	1795	if (v == v - 1.)
1389	return v; /* very large number */	1796	return v; /* very large numbers are assumed to be integer */
1390		1797
1391	f = shift * ev_floor (v * (1. / shift));	1798	f = shift * ev_floor (v * (1. / shift));
1392	return f + ev_floor (v - f);	1799	return f + ev_floor (v - f);
1393	}	1800	}
1394		1801
1395	/* special treatment for negative args? */
1396	if (expect_false (v < 0.))
1397	{
1398	ev_tstamp f = -ev_floor (-v);
1399
1400	return f - (f == v ? 0 : 1);
1401	}
1402
1403	/* fits into an unsigned long */	1802	/* fits into an unsigned long */
1404	return (unsigned long)v;	1803	return (unsigned long)v;
1405	}	1804	}
1406		1805
1407	#endif	1806	#endif
…		…
1410		1809
1411	#ifdef __linux	1810	#ifdef __linux
1412	# include <sys/utsname.h>	1811	# include <sys/utsname.h>
1413	#endif	1812	#endif
1414		1813
1415	static unsigned int noinline ecb_cold	1814	ecb_noinline ecb_cold
		1815	static unsigned int
1416	ev_linux_version (void)	1816	ev_linux_version (void)
1417	{	1817	{
1418	#ifdef __linux	1818	#ifdef __linux
1419	unsigned int v = 0;	1819	unsigned int v = 0;
1420	struct utsname buf;	1820	struct utsname buf;
…		…
1449	}	1849	}
1450		1850
1451	/*****************************************************************************/	1851	/*****************************************************************************/
1452		1852
1453	#if EV_AVOID_STDIO	1853	#if EV_AVOID_STDIO
1454	static void noinline ecb_cold	1854	ecb_noinline ecb_cold
		1855	static void
1455	ev_printerr (const char *msg)	1856	ev_printerr (const char *msg)
1456	{	1857	{
1457	write (STDERR_FILENO, msg, strlen (msg));	1858	write (STDERR_FILENO, msg, strlen (msg));
1458	}	1859	}
1459	#endif	1860	#endif
1460		1861
1461	static void (*syserr_cb)(const char *msg) EV_THROW;	1862	static void (*syserr_cb)(const char *msg) EV_NOEXCEPT;
1462		1863
1463	void ecb_cold	1864	ecb_cold
		1865	void
1464	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
1465	{	1867	{
1466	syserr_cb = cb;	1868	syserr_cb = cb;
1467	}	1869	}
1468		1870
1469	static void noinline ecb_cold	1871	ecb_noinline ecb_cold
		1872	static void
1470	ev_syserr (const char *msg)	1873	ev_syserr (const char *msg)
1471	{	1874	{
1472	if (!msg)	1875	if (!msg)
1473	msg = "(libev) system error";	1876	msg = "(libev) system error";
1474		1877
…		…
1487	abort ();	1890	abort ();
1488	}	1891	}
1489	}	1892	}
1490		1893
1491	static void *	1894	static void *
1492	ev_realloc_emul (void *ptr, long size) EV_THROW	1895	ev_realloc_emul (void *ptr, long size) EV_NOEXCEPT
1493	{	1896	{
1494	/* some systems, notably openbsd and darwin, fail to properly	1897	/* some systems, notably openbsd and darwin, fail to properly
1495	* 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
1496	* the single unix specification, so work around them here.	1899	* the single unix specification, so work around them here.
1497	* recently, also (at least) fedora and debian started breaking it,	1900	* recently, also (at least) fedora and debian started breaking it,
…		…
1503		1906
1504	free (ptr);	1907	free (ptr);
1505	return 0;	1908	return 0;
1506	}	1909	}
1507		1910
1508	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;
1509		1912
1510	void ecb_cold	1913	ecb_cold
		1914	void
1511	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
1512	{	1916	{
1513	alloc = cb;	1917	alloc = cb;
1514	}	1918	}
1515		1919
1516	inline_speed void *	1920	inline_speed void *
…		…
1543	typedef struct	1947	typedef struct
1544	{	1948	{
1545	WL head;	1949	WL head;
1546	unsigned char events; /* the events watched for */	1950	unsigned char events; /* the events watched for */
1547	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) */
1548	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 */
1549	unsigned char unused;	1953	unsigned char eflags; /* flags field for use by backends */
1550	#if EV_USE_EPOLL	1954	#if EV_USE_EPOLL
1551	unsigned int egen; /* generation counter to counter epoll bugs */	1955	unsigned int egen; /* generation counter to counter epoll bugs */
1552	#endif	1956	#endif
1553	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP	1957	#if EV_SELECT_IS_WINSOCKET || EV_USE_IOCP
1554	SOCKET handle;	1958	SOCKET handle;
…		…
1608	static struct ev_loop default_loop_struct;	2012	static struct ev_loop default_loop_struct;
1609	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 */
1610		2014
1611	#else	2015	#else
1612		2016
1613	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 */
1614	#define VAR(name,decl) static decl;	2018	#define VAR(name,decl) static decl;
1615	#include "ev_vars.h"	2019	#include "ev_vars.h"
1616	#undef VAR	2020	#undef VAR
1617		2021
1618	static int ev_default_loop_ptr;	2022	static int ev_default_loop_ptr;
1619		2023
1620	#endif	2024	#endif
1621		2025
1622	#if EV_FEATURE_API	2026	#if EV_FEATURE_API
1623	# 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)
1624	# 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)
1625	# define EV_INVOKE_PENDING invoke_cb (EV_A)	2029	# define EV_INVOKE_PENDING invoke_cb (EV_A)
1626	#else	2030	#else
1627	# define EV_RELEASE_CB (void)0	2031	# define EV_RELEASE_CB (void)0
1628	# define EV_ACQUIRE_CB (void)0	2032	# define EV_ACQUIRE_CB (void)0
1629	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)	2033	# define EV_INVOKE_PENDING ev_invoke_pending (EV_A)
…		…
1633		2037
1634	/*****************************************************************************/	2038	/*****************************************************************************/
1635		2039
1636	#ifndef EV_HAVE_EV_TIME	2040	#ifndef EV_HAVE_EV_TIME
1637	ev_tstamp	2041	ev_tstamp
1638	ev_time (void) EV_THROW	2042	ev_time (void) EV_NOEXCEPT
1639	{	2043	{
1640	#if EV_USE_REALTIME	2044	#if EV_USE_REALTIME
1641	if (expect_true (have_realtime))	2045	if (ecb_expect_true (have_realtime))
1642	{	2046	{
1643	struct timespec ts;	2047	struct timespec ts;
1644	clock_gettime (CLOCK_REALTIME, &ts);	2048	clock_gettime (CLOCK_REALTIME, &ts);
1645	return ts.tv_sec + ts.tv_nsec * 1e-9;	2049	return EV_TS_GET (ts);
1646	}	2050	}
1647	#endif	2051	#endif
1648		2052
		2053	{
1649	struct timeval tv;	2054	struct timeval tv;
1650	gettimeofday (&tv, 0);	2055	gettimeofday (&tv, 0);
1651	return tv.tv_sec + tv.tv_usec * 1e-6;	2056	return EV_TV_GET (tv);
		2057	}
1652	}	2058	}
1653	#endif	2059	#endif
1654		2060
1655	inline_size ev_tstamp	2061	inline_size ev_tstamp
1656	get_clock (void)	2062	get_clock (void)
1657	{	2063	{
1658	#if EV_USE_MONOTONIC	2064	#if EV_USE_MONOTONIC
1659	if (expect_true (have_monotonic))	2065	if (ecb_expect_true (have_monotonic))
1660	{	2066	{
1661	struct timespec ts;	2067	struct timespec ts;
1662	clock_gettime (CLOCK_MONOTONIC, &ts);	2068	clock_gettime (CLOCK_MONOTONIC, &ts);
1663	return ts.tv_sec + ts.tv_nsec * 1e-9;	2069	return EV_TS_GET (ts);
1664	}	2070	}
1665	#endif	2071	#endif
1666		2072
1667	return ev_time ();	2073	return ev_time ();
1668	}	2074	}
1669		2075
1670	#if EV_MULTIPLICITY	2076	#if EV_MULTIPLICITY
1671	ev_tstamp	2077	ev_tstamp
1672	ev_now (EV_P) EV_THROW	2078	ev_now (EV_P) EV_NOEXCEPT
1673	{	2079	{
1674	return ev_rt_now;	2080	return ev_rt_now;
1675	}	2081	}
1676	#endif	2082	#endif
1677		2083
1678	void	2084	void
1679	ev_sleep (ev_tstamp delay) EV_THROW	2085	ev_sleep (ev_tstamp delay) EV_NOEXCEPT
1680	{	2086	{
1681	if (delay > 0.)	2087	if (delay > EV_TS_CONST (0.))
1682	{	2088	{
1683	#if EV_USE_NANOSLEEP	2089	#if EV_USE_NANOSLEEP
1684	struct timespec ts;	2090	struct timespec ts;
1685		2091
1686	EV_TS_SET (ts, delay);	2092	EV_TS_SET (ts, delay);
1687	nanosleep (&ts, 0);	2093	nanosleep (&ts, 0);
1688	#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) */
1689	Sleep ((unsigned long)(delay * 1e3));	2097	Sleep ((unsigned long)(EV_TS_TO_MSEC (delay)));
1690	#else	2098	#else
1691	struct timeval tv;	2099	struct timeval tv;
1692		2100
1693	/* 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 */
1694	/* something not guaranteed by newer posix versions, but guaranteed */	2102	/* something not guaranteed by newer posix versions, but guaranteed */
…		…
1724	}	2132	}
1725		2133
1726	return ncur;	2134	return ncur;
1727	}	2135	}
1728		2136
1729	static void * noinline ecb_cold	2137	ecb_noinline ecb_cold
		2138	static void *
1730	array_realloc (int elem, void *base, int *cur, int cnt)	2139	array_realloc (int elem, void *base, int *cur, int cnt)
1731	{	2140	{
1732	*cur = array_nextsize (elem, *cur, cnt);	2141	*cur = array_nextsize (elem, *cur, cnt);
1733	return ev_realloc (base, elem * *cur);	2142	return ev_realloc (base, elem * *cur);
1734	}	2143	}
1735		2144
		2145	#define array_needsize_noinit(base,offset,count)
		2146
1736	#define array_init_zero(base,count) \	2147	#define array_needsize_zerofill(base,offset,count) \
1737	memset ((void *)(base), 0, sizeof (*(base)) * (count))	2148	memset ((void *)(base + offset), 0, sizeof (*(base)) * (count))
1738		2149
1739	#define array_needsize(type,base,cur,cnt,init) \	2150	#define array_needsize(type,base,cur,cnt,init) \
1740	if (expect_false ((cnt) > (cur))) \	2151	if (ecb_expect_false ((cnt) > (cur))) \
1741	{ \	2152	{ \
1742	int ecb_unused ocur_ = (cur); \	2153	ecb_unused int ocur_ = (cur); \
1743	(base) = (type *)array_realloc \	2154	(base) = (type *)array_realloc \
1744	(sizeof (type), (base), &(cur), (cnt)); \	2155	(sizeof (type), (base), &(cur), (cnt)); \
1745	init ((base) + (ocur_), (cur) - ocur_); \	2156	init ((base), ocur_, ((cur) - ocur_)); \
1746	}	2157	}
1747		2158
1748	#if 0	2159	#if 0
1749	#define array_slim(type,stem) \	2160	#define array_slim(type,stem) \
1750	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \	2161	if (stem ## max < array_roundsize (stem ## cnt >> 2)) \
…		…
1759	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
1760		2171
1761	/*****************************************************************************/	2172	/*****************************************************************************/
1762		2173
1763	/* dummy callback for pending events */	2174	/* dummy callback for pending events */
1764	static void noinline	2175	ecb_noinline
		2176	static void
1765	pendingcb (EV_P_ ev_prepare *w, int revents)	2177	pendingcb (EV_P_ ev_prepare *w, int revents)
1766	{	2178	{
1767	}	2179	}
1768		2180
1769	void noinline	2181	ecb_noinline
		2182	void
1770	ev_feed_event (EV_P_ void *w, int revents) EV_THROW	2183	ev_feed_event (EV_P_ void *w, int revents) EV_NOEXCEPT
1771	{	2184	{
1772	W w_ = (W)w;	2185	W w_ = (W)w;
1773	int pri = ABSPRI (w_);	2186	int pri = ABSPRI (w_);
1774		2187
1775	if (expect_false (w_->pending))	2188	if (ecb_expect_false (w_->pending))
1776	pendings [pri][w_->pending - 1].events |= revents;	2189	pendings [pri][w_->pending - 1].events |= revents;
1777	else	2190	else
1778	{	2191	{
1779	w_->pending = ++pendingcnt [pri];	2192	w_->pending = ++pendingcnt [pri];
1780	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, EMPTY2);	2193	array_needsize (ANPENDING, pendings [pri], pendingmax [pri], w_->pending, array_needsize_noinit);
1781	pendings [pri][w_->pending - 1].w = w_;	2194	pendings [pri][w_->pending - 1].w = w_;
1782	pendings [pri][w_->pending - 1].events = revents;	2195	pendings [pri][w_->pending - 1].events = revents;
1783	}	2196	}
1784		2197
1785	pendingpri = NUMPRI - 1;	2198	pendingpri = NUMPRI - 1;
1786	}	2199	}
1787		2200
1788	inline_speed void	2201	inline_speed void
1789	feed_reverse (EV_P_ W w)	2202	feed_reverse (EV_P_ W w)
1790	{	2203	{
1791	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, EMPTY2);	2204	array_needsize (W, rfeeds, rfeedmax, rfeedcnt + 1, array_needsize_noinit);
1792	rfeeds [rfeedcnt++] = w;	2205	rfeeds [rfeedcnt++] = w;
1793	}	2206	}
1794		2207
1795	inline_size void	2208	inline_size void
1796	feed_reverse_done (EV_P_ int revents)	2209	feed_reverse_done (EV_P_ int revents)
…		…
1831	inline_speed void	2244	inline_speed void
1832	fd_event (EV_P_ int fd, int revents)	2245	fd_event (EV_P_ int fd, int revents)
1833	{	2246	{
1834	ANFD *anfd = anfds + fd;	2247	ANFD *anfd = anfds + fd;
1835		2248
1836	if (expect_true (!anfd->reify))	2249	if (ecb_expect_true (!anfd->reify))
1837	fd_event_nocheck (EV_A_ fd, revents);	2250	fd_event_nocheck (EV_A_ fd, revents);
1838	}	2251	}
1839		2252
1840	void	2253	void
1841	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
1842	{	2255	{
1843	if (fd >= 0 && fd < anfdmax)	2256	if (fd >= 0 && fd < anfdmax)
1844	fd_event_nocheck (EV_A_ fd, revents);	2257	fd_event_nocheck (EV_A_ fd, revents);
1845	}	2258	}
1846		2259
…		…
1883	ev_io *w;	2296	ev_io *w;
1884		2297
1885	unsigned char o_events = anfd->events;	2298	unsigned char o_events = anfd->events;
1886	unsigned char o_reify = anfd->reify;	2299	unsigned char o_reify = anfd->reify;
1887		2300
1888	anfd->reify = 0;	2301	anfd->reify = 0;
1889		2302
1890	/*if (expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */	2303	/*if (ecb_expect_true (o_reify & EV_ANFD_REIFY)) probably a deoptimisation */
1891	{	2304	{
1892	anfd->events = 0;	2305	anfd->events = 0;
1893		2306
1894	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)	2307	for (w = (ev_io *)anfd->head; w; w = (ev_io *)((WL)w)->next)
1895	anfd->events |= (unsigned char)w->events;	2308	anfd->events |= (unsigned char)w->events;
…		…
1904		2317
1905	fdchangecnt = 0;	2318	fdchangecnt = 0;
1906	}	2319	}
1907		2320
1908	/* something about the given fd changed */	2321	/* something about the given fd changed */
1909	inline_size void	2322	inline_size
		2323	void
1910	fd_change (EV_P_ int fd, int flags)	2324	fd_change (EV_P_ int fd, int flags)
1911	{	2325	{
1912	unsigned char reify = anfds [fd].reify;	2326	unsigned char reify = anfds [fd].reify;
1913	anfds [fd].reify |= flags;	2327	anfds [fd].reify |= flags;
1914		2328
1915	if (expect_true (!reify))	2329	if (ecb_expect_true (!reify))
1916	{	2330	{
1917	++fdchangecnt;	2331	++fdchangecnt;
1918	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, EMPTY2);	2332	array_needsize (int, fdchanges, fdchangemax, fdchangecnt, array_needsize_noinit);
1919	fdchanges [fdchangecnt - 1] = fd;	2333	fdchanges [fdchangecnt - 1] = fd;
1920	}	2334	}
1921	}	2335	}
1922		2336
1923	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */	2337	/* the given fd is invalid/unusable, so make sure it doesn't hurt us anymore */
1924	inline_speed void ecb_cold	2338	inline_speed ecb_cold void
1925	fd_kill (EV_P_ int fd)	2339	fd_kill (EV_P_ int fd)
1926	{	2340	{
1927	ev_io *w;	2341	ev_io *w;
1928		2342
1929	while ((w = (ev_io *)anfds [fd].head))	2343	while ((w = (ev_io *)anfds [fd].head))
…		…
1932	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);	2346	ev_feed_event (EV_A_ (W)w, EV_ERROR | EV_READ | EV_WRITE);
1933	}	2347	}
1934	}	2348	}
1935		2349
1936	/* check whether the given fd is actually valid, for error recovery */	2350	/* check whether the given fd is actually valid, for error recovery */
1937	inline_size int ecb_cold	2351	inline_size ecb_cold int
1938	fd_valid (int fd)	2352	fd_valid (int fd)
1939	{	2353	{
1940	#ifdef _WIN32	2354	#ifdef _WIN32
1941	return EV_FD_TO_WIN32_HANDLE (fd) != -1;	2355	return EV_FD_TO_WIN32_HANDLE (fd) != -1;
1942	#else	2356	#else
1943	return fcntl (fd, F_GETFD) != -1;	2357	return fcntl (fd, F_GETFD) != -1;
1944	#endif	2358	#endif
1945	}	2359	}
1946		2360
1947	/* called on EBADF to verify fds */	2361	/* called on EBADF to verify fds */
1948	static void noinline ecb_cold	2362	ecb_noinline ecb_cold
		2363	static void
1949	fd_ebadf (EV_P)	2364	fd_ebadf (EV_P)
1950	{	2365	{
1951	int fd;	2366	int fd;
1952		2367
1953	for (fd = 0; fd < anfdmax; ++fd)	2368	for (fd = 0; fd < anfdmax; ++fd)
…		…
1955	if (!fd_valid (fd) && errno == EBADF)	2370	if (!fd_valid (fd) && errno == EBADF)
1956	fd_kill (EV_A_ fd);	2371	fd_kill (EV_A_ fd);
1957	}	2372	}
1958		2373
1959	/* called on ENOMEM in select/poll to kill some fds and retry */	2374	/* called on ENOMEM in select/poll to kill some fds and retry */
1960	static void noinline ecb_cold	2375	ecb_noinline ecb_cold
		2376	static void
1961	fd_enomem (EV_P)	2377	fd_enomem (EV_P)
1962	{	2378	{
1963	int fd;	2379	int fd;
1964		2380
1965	for (fd = anfdmax; fd--; )	2381	for (fd = anfdmax; fd--; )
…		…
1969	break;	2385	break;
1970	}	2386	}
1971	}	2387	}
1972		2388
1973	/* usually called after fork if backend needs to re-arm all fds from scratch */	2389	/* usually called after fork if backend needs to re-arm all fds from scratch */
1974	static void noinline	2390	ecb_noinline
		2391	static void
1975	fd_rearm_all (EV_P)	2392	fd_rearm_all (EV_P)
1976	{	2393	{
1977	int fd;	2394	int fd;
1978		2395
1979	for (fd = 0; fd < anfdmax; ++fd)	2396	for (fd = 0; fd < anfdmax; ++fd)
…		…
2032	ev_tstamp minat;	2449	ev_tstamp minat;
2033	ANHE *minpos;	2450	ANHE *minpos;
2034	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;	2451	ANHE *pos = heap + DHEAP * (k - HEAP0) + HEAP0 + 1;
2035		2452
2036	/* find minimum child */	2453	/* find minimum child */
2037	if (expect_true (pos + DHEAP - 1 < E))	2454	if (ecb_expect_true (pos + DHEAP - 1 < E))
2038	{	2455	{
2039	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));	2456	/* fast path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));
2040	if ( ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));	2457	if ( minat > ANHE_at (pos [1])) (minpos = pos + 1), (minat = ANHE_at (*minpos));
2041	if ( ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));	2458	if ( minat > ANHE_at (pos [2])) (minpos = pos + 2), (minat = ANHE_at (*minpos));
2042	if ( ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));	2459	if ( minat > ANHE_at (pos [3])) (minpos = pos + 3), (minat = ANHE_at (*minpos));
2043	}	2460	}
2044	else if (pos < E)	2461	else if (pos < E)
2045	{	2462	{
2046	/* slow path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));	2463	/* slow path */ (minpos = pos + 0), (minat = ANHE_at (*minpos));
2047	if (pos + 1 < E && ANHE_at (pos [1]) < minat) (minpos = pos + 1), (minat = ANHE_at (*minpos));	2464	if (pos + 1 < E && minat > ANHE_at (pos [1])) (minpos = pos + 1), (minat = ANHE_at (*minpos));
2048	if (pos + 2 < E && ANHE_at (pos [2]) < minat) (minpos = pos + 2), (minat = ANHE_at (*minpos));	2465	if (pos + 2 < E && minat > ANHE_at (pos [2])) (minpos = pos + 2), (minat = ANHE_at (*minpos));
2049	if (pos + 3 < E && ANHE_at (pos [3]) < minat) (minpos = pos + 3), (minat = ANHE_at (*minpos));	2466	if (pos + 3 < E && minat > ANHE_at (pos [3])) (minpos = pos + 3), (minat = ANHE_at (*minpos));
2050	}	2467	}
2051	else	2468	else
2052	break;	2469	break;
2053		2470
2054	if (ANHE_at (he) <= minat)	2471	if (ANHE_at (he) <= minat)
…		…
2062		2479
2063	heap [k] = he;	2480	heap [k] = he;
2064	ev_active (ANHE_w (he)) = k;	2481	ev_active (ANHE_w (he)) = k;
2065	}	2482	}
2066		2483
2067	#else /* 4HEAP */	2484	#else /* not 4HEAP */
2068		2485
2069	#define HEAP0 1	2486	#define HEAP0 1
2070	#define HPARENT(k) ((k) >> 1)	2487	#define HPARENT(k) ((k) >> 1)
2071	#define UPHEAP_DONE(p,k) (!(p))	2488	#define UPHEAP_DONE(p,k) (!(p))
2072		2489
…		…
2160		2577
2161	/*****************************************************************************/	2578	/*****************************************************************************/
2162		2579
2163	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	2580	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2164		2581
2165	static void noinline ecb_cold	2582	ecb_noinline ecb_cold
		2583	static void
2166	evpipe_init (EV_P)	2584	evpipe_init (EV_P)
2167	{	2585	{
2168	if (!ev_is_active (&pipe_w))	2586	if (!ev_is_active (&pipe_w))
2169	{	2587	{
2170	int fds [2];	2588	int fds [2];
…		…
2210	inline_speed void	2628	inline_speed void
2211	evpipe_write (EV_P_ EV_ATOMIC_T *flag)	2629	evpipe_write (EV_P_ EV_ATOMIC_T *flag)
2212	{	2630	{
2213	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */	2631	ECB_MEMORY_FENCE; /* push out the write before this function was called, acquire flag */
2214		2632
2215	if (expect_true (*flag))	2633	if (ecb_expect_true (*flag))
2216	return;	2634	return;
2217		2635
2218	*flag = 1;	2636	*flag = 1;
2219	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */	2637	ECB_MEMORY_FENCE_RELEASE; /* make sure flag is visible before the wakeup */
2220		2638
…		…
2241	#endif	2659	#endif
2242	{	2660	{
2243	#ifdef _WIN32	2661	#ifdef _WIN32
2244	WSABUF buf;	2662	WSABUF buf;
2245	DWORD sent;	2663	DWORD sent;
2246	buf.buf = &buf;	2664	buf.buf = (char *)&buf;
2247	buf.len = 1;	2665	buf.len = 1;
2248	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);	2666	WSASend (EV_FD_TO_WIN32_HANDLE (evpipe [1]), &buf, 1, &sent, 0, 0, 0);
2249	#else	2667	#else
2250	write (evpipe [1], &(evpipe [1]), 1);	2668	write (evpipe [1], &(evpipe [1]), 1);
2251	#endif	2669	#endif
…		…
2297	sig_pending = 0;	2715	sig_pending = 0;
2298		2716
2299	ECB_MEMORY_FENCE;	2717	ECB_MEMORY_FENCE;
2300		2718
2301	for (i = EV_NSIG - 1; i--; )	2719	for (i = EV_NSIG - 1; i--; )
2302	if (expect_false (signals [i].pending))	2720	if (ecb_expect_false (signals [i].pending))
2303	ev_feed_signal_event (EV_A_ i + 1);	2721	ev_feed_signal_event (EV_A_ i + 1);
2304	}	2722	}
2305	#endif	2723	#endif
2306		2724
2307	#if EV_ASYNC_ENABLE	2725	#if EV_ASYNC_ENABLE
…		…
2323	}	2741	}
2324		2742
2325	/*****************************************************************************/	2743	/*****************************************************************************/
2326		2744
2327	void	2745	void
2328	ev_feed_signal (int signum) EV_THROW	2746	ev_feed_signal (int signum) EV_NOEXCEPT
2329	{	2747	{
2330	#if EV_MULTIPLICITY	2748	#if EV_MULTIPLICITY
2331	EV_P;	2749	EV_P;
2332	ECB_MEMORY_FENCE_ACQUIRE;	2750	ECB_MEMORY_FENCE_ACQUIRE;
2333	EV_A = signals [signum - 1].loop;	2751	EV_A = signals [signum - 1].loop;
…		…
2348	#endif	2766	#endif
2349		2767
2350	ev_feed_signal (signum);	2768	ev_feed_signal (signum);
2351	}	2769	}
2352		2770
2353	void noinline	2771	ecb_noinline
		2772	void
2354	ev_feed_signal_event (EV_P_ int signum) EV_THROW	2773	ev_feed_signal_event (EV_P_ int signum) EV_NOEXCEPT
2355	{	2774	{
2356	WL w;	2775	WL w;
2357		2776
2358	if (expect_false (signum <= 0 || signum >= EV_NSIG))	2777	if (ecb_expect_false (signum <= 0 || signum >= EV_NSIG))
2359	return;	2778	return;
2360		2779
2361	--signum;	2780	--signum;
2362		2781
2363	#if EV_MULTIPLICITY	2782	#if EV_MULTIPLICITY
2364	/* it is permissible to try to feed a signal to the wrong loop */	2783	/* it is permissible to try to feed a signal to the wrong loop */
2365	/* or, likely more useful, feeding a signal nobody is waiting for */	2784	/* or, likely more useful, feeding a signal nobody is waiting for */
2366		2785
2367	if (expect_false (signals [signum].loop != EV_A))	2786	if (ecb_expect_false (signals [signum].loop != EV_A))
2368	return;	2787	return;
2369	#endif	2788	#endif
2370		2789
2371	signals [signum].pending = 0;	2790	signals [signum].pending = 0;
2372	ECB_MEMORY_FENCE_RELEASE;	2791	ECB_MEMORY_FENCE_RELEASE;
…		…
2456		2875
2457	#endif	2876	#endif
2458		2877
2459	/*****************************************************************************/	2878	/*****************************************************************************/
2460		2879
		2880	#if EV_USE_TIMERFD
		2881
		2882	static void periodics_reschedule (EV_P);
		2883
		2884	static void
		2885	timerfdcb (EV_P_ ev_io *iow, int revents)
		2886	{
		2887	struct itimerspec its = { 0 };
		2888
		2889	/* since we can't easily come zup with a (portable) maximum value of time_t,
		2890	* we wake up once per month, which hopefully is rare enough to not
		2891	* be a problem. */
		2892	its.it_value.tv_sec = ev_rt_now + 86400 * 30;
		2893	timerfd_settime (timerfd, TFD_TIMER_ABSTIME | TFD_TIMER_CANCEL_ON_SET, &its, 0);
		2894
		2895	ev_rt_now = ev_time ();
		2896	/* periodics_reschedule only needs ev_rt_now */
		2897	/* but maybe in the future we want the full treatment. */
		2898	/*
		2899	now_floor = EV_TS_CONST (0.);
		2900	time_update (EV_A_ EV_TSTAMP_HUGE);
		2901	*/
		2902	periodics_reschedule (EV_A);
		2903	}
		2904
		2905	ecb_noinline ecb_cold
		2906	static void
		2907	evtimerfd_init (EV_P)
		2908	{
		2909	if (!ev_is_active (&timerfd_w))
		2910	{
		2911	timerfd = timerfd_create (CLOCK_REALTIME, TFD_NONBLOCK | TFD_CLOEXEC);
		2912
		2913	if (timerfd >= 0)
		2914	{
		2915	fd_intern (timerfd); /* just to be sure */
		2916
		2917	ev_io_init (&timerfd_w, timerfdcb, timerfd, EV_READ);
		2918	ev_set_priority (&sigfd_w, EV_MINPRI);
		2919	ev_io_start (EV_A_ &timerfd_w);
		2920	ev_unref (EV_A); /* watcher should not keep loop alive */
		2921
		2922	/* (re-) arm timer */
		2923	timerfdcb (EV_A_ 0, 0);
		2924	}
		2925	}
		2926	}
		2927
		2928	#endif
		2929
		2930	/*****************************************************************************/
		2931
2461	#if EV_USE_IOCP	2932	#if EV_USE_IOCP
2462	# include "ev_iocp.c"	2933	# include "ev_iocp.c"
2463	#endif	2934	#endif
2464	#if EV_USE_PORT	2935	#if EV_USE_PORT
2465	# include "ev_port.c"	2936	# include "ev_port.c"
…		…
2468	# include "ev_kqueue.c"	2939	# include "ev_kqueue.c"
2469	#endif	2940	#endif
2470	#if EV_USE_EPOLL	2941	#if EV_USE_EPOLL
2471	# include "ev_epoll.c"	2942	# include "ev_epoll.c"
2472	#endif	2943	#endif
		2944	#if EV_USE_LINUXAIO
		2945	# include "ev_linuxaio.c"
		2946	#endif
		2947	#if EV_USE_IOURING
		2948	# include "ev_iouring.c"
		2949	#endif
2473	#if EV_USE_POLL	2950	#if EV_USE_POLL
2474	# include "ev_poll.c"	2951	# include "ev_poll.c"
2475	#endif	2952	#endif
2476	#if EV_USE_SELECT	2953	#if EV_USE_SELECT
2477	# include "ev_select.c"	2954	# include "ev_select.c"
2478	#endif	2955	#endif
2479		2956
2480	int ecb_cold	2957	ecb_cold int
2481	ev_version_major (void) EV_THROW	2958	ev_version_major (void) EV_NOEXCEPT
2482	{	2959	{
2483	return EV_VERSION_MAJOR;	2960	return EV_VERSION_MAJOR;
2484	}	2961	}
2485		2962
2486	int ecb_cold	2963	ecb_cold int
2487	ev_version_minor (void) EV_THROW	2964	ev_version_minor (void) EV_NOEXCEPT
2488	{	2965	{
2489	return EV_VERSION_MINOR;	2966	return EV_VERSION_MINOR;
2490	}	2967	}
2491		2968
2492	/* return true if we are running with elevated privileges and should ignore env variables */	2969	/* return true if we are running with elevated privileges and should ignore env variables */
2493	int inline_size ecb_cold	2970	inline_size ecb_cold int
2494	enable_secure (void)	2971	enable_secure (void)
2495	{	2972	{
2496	#ifdef _WIN32	2973	#ifdef _WIN32
2497	return 0;	2974	return 0;
2498	#else	2975	#else
2499	return getuid () != geteuid ()	2976	return getuid () != geteuid ()
2500	|| getgid () != getegid ();	2977	|| getgid () != getegid ();
2501	#endif	2978	#endif
2502	}	2979	}
2503		2980
2504	unsigned int ecb_cold	2981	ecb_cold
		2982	unsigned int
2505	ev_supported_backends (void) EV_THROW	2983	ev_supported_backends (void) EV_NOEXCEPT
2506	{	2984	{
2507	unsigned int flags = 0;	2985	unsigned int flags = 0;
2508		2986
2509	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;	2987	if (EV_USE_PORT ) flags |= EVBACKEND_PORT;
2510	if (EV_USE_KQUEUE) flags |= EVBACKEND_KQUEUE;	2988	if (EV_USE_KQUEUE ) flags |= EVBACKEND_KQUEUE;
2511	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;	2989	if (EV_USE_EPOLL ) flags |= EVBACKEND_EPOLL;
		2990	if (EV_USE_LINUXAIO) flags |= EVBACKEND_LINUXAIO;
		2991	if (EV_USE_IOURING ) flags |= EVBACKEND_IOURING;
2512	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;	2992	if (EV_USE_POLL ) flags |= EVBACKEND_POLL;
2513	if (EV_USE_SELECT) flags |= EVBACKEND_SELECT;	2993	if (EV_USE_SELECT ) flags |= EVBACKEND_SELECT;
2514		2994
2515	return flags;	2995	return flags;
2516	}	2996	}
2517		2997
2518	unsigned int ecb_cold	2998	ecb_cold
		2999	unsigned int
2519	ev_recommended_backends (void) EV_THROW	3000	ev_recommended_backends (void) EV_NOEXCEPT
2520	{	3001	{
2521	unsigned int flags = ev_supported_backends ();	3002	unsigned int flags = ev_supported_backends ();
2522		3003
2523	#ifndef __NetBSD__	3004	#ifndef __NetBSD__
2524	/* kqueue is borked on everything but netbsd apparently */	3005	/* kqueue is borked on everything but netbsd apparently */
…		…
2532	#endif	3013	#endif
2533	#ifdef __FreeBSD__	3014	#ifdef __FreeBSD__
2534	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */	3015	flags &= ~EVBACKEND_POLL; /* poll return value is unusable (http://forums.freebsd.org/archive/index.php/t-10270.html) */
2535	#endif	3016	#endif
2536		3017
		3018	/* TODO: linuxaio is very experimental */
		3019	#if !EV_RECOMMEND_LINUXAIO
		3020	flags &= ~EVBACKEND_LINUXAIO;
		3021	#endif
		3022	/* TODO: linuxaio is super experimental */
		3023	#if !EV_RECOMMEND_IOURING
		3024	flags &= ~EVBACKEND_IOURING;
		3025	#endif
		3026
2537	return flags;	3027	return flags;
2538	}	3028	}
2539		3029
2540	unsigned int ecb_cold	3030	ecb_cold
		3031	unsigned int
2541	ev_embeddable_backends (void) EV_THROW	3032	ev_embeddable_backends (void) EV_NOEXCEPT
2542	{	3033	{
2543	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;	3034	int flags = EVBACKEND_EPOLL | EVBACKEND_KQUEUE | EVBACKEND_PORT;
2544		3035
2545	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */	3036	/* epoll embeddability broken on all linux versions up to at least 2.6.23 */
2546	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */	3037	if (ev_linux_version () < 0x020620) /* disable it on linux < 2.6.32 */
2547	flags &= ~EVBACKEND_EPOLL;	3038	flags &= ~EVBACKEND_EPOLL;
2548		3039
		3040	/* EVBACKEND_LINUXAIO is theoretically embeddable, but suffers from a performance overhead */
		3041
		3042	/* EVBACKEND_IOURING is practically embeddable, but the current implementation is not
		3043	* because our backend_fd is the epoll fd we need as fallback.
		3044	* if the kernel ever is fixed, this might change...
		3045	*/
		3046
2549	return flags;	3047	return flags;
2550	}	3048	}
2551		3049
2552	unsigned int	3050	unsigned int
2553	ev_backend (EV_P) EV_THROW	3051	ev_backend (EV_P) EV_NOEXCEPT
2554	{	3052	{
2555	return backend;	3053	return backend;
2556	}	3054	}
2557		3055
2558	#if EV_FEATURE_API	3056	#if EV_FEATURE_API
2559	unsigned int	3057	unsigned int
2560	ev_iteration (EV_P) EV_THROW	3058	ev_iteration (EV_P) EV_NOEXCEPT
2561	{	3059	{
2562	return loop_count;	3060	return loop_count;
2563	}	3061	}
2564		3062
2565	unsigned int	3063	unsigned int
2566	ev_depth (EV_P) EV_THROW	3064	ev_depth (EV_P) EV_NOEXCEPT
2567	{	3065	{
2568	return loop_depth;	3066	return loop_depth;
2569	}	3067	}
2570		3068
2571	void	3069	void
2572	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	3070	ev_set_io_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2573	{	3071	{
2574	io_blocktime = interval;	3072	io_blocktime = interval;
2575	}	3073	}
2576		3074
2577	void	3075	void
2578	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_THROW	3076	ev_set_timeout_collect_interval (EV_P_ ev_tstamp interval) EV_NOEXCEPT
2579	{	3077	{
2580	timeout_blocktime = interval;	3078	timeout_blocktime = interval;
2581	}	3079	}
2582		3080
2583	void	3081	void
2584	ev_set_userdata (EV_P_ void *data) EV_THROW	3082	ev_set_userdata (EV_P_ void *data) EV_NOEXCEPT
2585	{	3083	{
2586	userdata = data;	3084	userdata = data;
2587	}	3085	}
2588		3086
2589	void *	3087	void *
2590	ev_userdata (EV_P) EV_THROW	3088	ev_userdata (EV_P) EV_NOEXCEPT
2591	{	3089	{
2592	return userdata;	3090	return userdata;
2593	}	3091	}
2594		3092
2595	void	3093	void
2596	ev_set_invoke_pending_cb (EV_P_ ev_loop_callback invoke_pending_cb) EV_THROW	3094	ev_set_invoke_pending_cb (EV_P_ ev_loop_callback invoke_pending_cb) EV_NOEXCEPT
2597	{	3095	{
2598	invoke_cb = invoke_pending_cb;	3096	invoke_cb = invoke_pending_cb;
2599	}	3097	}
2600		3098
2601	void	3099	void
2602	ev_set_loop_release_cb (EV_P_ ev_loop_callback_nothrow release, ev_loop_callback_nothrow acquire) EV_THROW	3100	ev_set_loop_release_cb (EV_P_ void (*release)(EV_P) EV_NOEXCEPT, void (*acquire)(EV_P) EV_NOEXCEPT) EV_NOEXCEPT
2603	{	3101	{
2604	release_cb = release;	3102	release_cb = release;
2605	acquire_cb = acquire;	3103	acquire_cb = acquire;
2606	}	3104	}
2607	#endif	3105	#endif
2608		3106
2609	/* initialise a loop structure, must be zero-initialised */	3107	/* initialise a loop structure, must be zero-initialised */
2610	static void noinline ecb_cold	3108	ecb_noinline ecb_cold
		3109	static void
2611	loop_init (EV_P_ unsigned int flags) EV_THROW	3110	loop_init (EV_P_ unsigned int flags) EV_NOEXCEPT
2612	{	3111	{
2613	if (!backend)	3112	if (!backend)
2614	{	3113	{
2615	origflags = flags;	3114	origflags = flags;
2616		3115
…		…
2669	fs_fd = flags & EVFLAG_NOINOTIFY ? -1 : -2;	3168	fs_fd = flags & EVFLAG_NOINOTIFY ? -1 : -2;
2670	#endif	3169	#endif
2671	#if EV_USE_SIGNALFD	3170	#if EV_USE_SIGNALFD
2672	sigfd = flags & EVFLAG_SIGNALFD ? -2 : -1;	3171	sigfd = flags & EVFLAG_SIGNALFD ? -2 : -1;
2673	#endif	3172	#endif
		3173	#if EV_USE_TIMERFD
		3174	timerfd = flags & EVFLAG_NOTIMERFD ? -1 : -2;
		3175	#endif
2674		3176
2675	if (!(flags & EVBACKEND_MASK))	3177	if (!(flags & EVBACKEND_MASK))
2676	flags |= ev_recommended_backends ();	3178	flags |= ev_recommended_backends ();
2677		3179
2678	#if EV_USE_IOCP	3180	#if EV_USE_IOCP
2679	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);	3181	if (!backend && (flags & EVBACKEND_IOCP )) backend = iocp_init (EV_A_ flags);
2680	#endif	3182	#endif
2681	#if EV_USE_PORT	3183	#if EV_USE_PORT
2682	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);	3184	if (!backend && (flags & EVBACKEND_PORT )) backend = port_init (EV_A_ flags);
2683	#endif	3185	#endif
2684	#if EV_USE_KQUEUE	3186	#if EV_USE_KQUEUE
2685	if (!backend && (flags & EVBACKEND_KQUEUE)) backend = kqueue_init (EV_A_ flags);	3187	if (!backend && (flags & EVBACKEND_KQUEUE )) backend = kqueue_init (EV_A_ flags);
		3188	#endif
		3189	#if EV_USE_IOURING
		3190	if (!backend && (flags & EVBACKEND_IOURING )) backend = iouring_init (EV_A_ flags);
		3191	#endif
		3192	#if EV_USE_LINUXAIO
		3193	if (!backend && (flags & EVBACKEND_LINUXAIO)) backend = linuxaio_init (EV_A_ flags);
2686	#endif	3194	#endif
2687	#if EV_USE_EPOLL	3195	#if EV_USE_EPOLL
2688	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);	3196	if (!backend && (flags & EVBACKEND_EPOLL )) backend = epoll_init (EV_A_ flags);
2689	#endif	3197	#endif
2690	#if EV_USE_POLL	3198	#if EV_USE_POLL
2691	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);	3199	if (!backend && (flags & EVBACKEND_POLL )) backend = poll_init (EV_A_ flags);
2692	#endif	3200	#endif
2693	#if EV_USE_SELECT	3201	#if EV_USE_SELECT
2694	if (!backend && (flags & EVBACKEND_SELECT)) backend = select_init (EV_A_ flags);	3202	if (!backend && (flags & EVBACKEND_SELECT )) backend = select_init (EV_A_ flags);
2695	#endif	3203	#endif
2696		3204
2697	ev_prepare_init (&pending_w, pendingcb);	3205	ev_prepare_init (&pending_w, pendingcb);
2698		3206
2699	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	3207	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
…		…
2702	#endif	3210	#endif
2703	}	3211	}
2704	}	3212	}
2705		3213
2706	/* free up a loop structure */	3214	/* free up a loop structure */
2707	void ecb_cold	3215	ecb_cold
		3216	void
2708	ev_loop_destroy (EV_P)	3217	ev_loop_destroy (EV_P)
2709	{	3218	{
2710	int i;	3219	int i;
2711		3220
2712	#if EV_MULTIPLICITY	3221	#if EV_MULTIPLICITY
…		…
2715	return;	3224	return;
2716	#endif	3225	#endif
2717		3226
2718	#if EV_CLEANUP_ENABLE	3227	#if EV_CLEANUP_ENABLE
2719	/* queue cleanup watchers (and execute them) */	3228	/* queue cleanup watchers (and execute them) */
2720	if (expect_false (cleanupcnt))	3229	if (ecb_expect_false (cleanupcnt))
2721	{	3230	{
2722	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);	3231	queue_events (EV_A_ (W *)cleanups, cleanupcnt, EV_CLEANUP);
2723	EV_INVOKE_PENDING;	3232	EV_INVOKE_PENDING;
2724	}	3233	}
2725	#endif	3234	#endif
…		…
2744	#if EV_USE_SIGNALFD	3253	#if EV_USE_SIGNALFD
2745	if (ev_is_active (&sigfd_w))	3254	if (ev_is_active (&sigfd_w))
2746	close (sigfd);	3255	close (sigfd);
2747	#endif	3256	#endif
2748		3257
		3258	#if EV_USE_TIMERFD
		3259	if (ev_is_active (&timerfd_w))
		3260	close (timerfd);
		3261	#endif
		3262
2749	#if EV_USE_INOTIFY	3263	#if EV_USE_INOTIFY
2750	if (fs_fd >= 0)	3264	if (fs_fd >= 0)
2751	close (fs_fd);	3265	close (fs_fd);
2752	#endif	3266	#endif
2753		3267
2754	if (backend_fd >= 0)	3268	if (backend_fd >= 0)
2755	close (backend_fd);	3269	close (backend_fd);
2756		3270
2757	#if EV_USE_IOCP	3271	#if EV_USE_IOCP
2758	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);	3272	if (backend == EVBACKEND_IOCP ) iocp_destroy (EV_A);
2759	#endif	3273	#endif
2760	#if EV_USE_PORT	3274	#if EV_USE_PORT
2761	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);	3275	if (backend == EVBACKEND_PORT ) port_destroy (EV_A);
2762	#endif	3276	#endif
2763	#if EV_USE_KQUEUE	3277	#if EV_USE_KQUEUE
2764	if (backend == EVBACKEND_KQUEUE) kqueue_destroy (EV_A);	3278	if (backend == EVBACKEND_KQUEUE ) kqueue_destroy (EV_A);
		3279	#endif
		3280	#if EV_USE_IOURING
		3281	if (backend == EVBACKEND_IOURING ) iouring_destroy (EV_A);
		3282	#endif
		3283	#if EV_USE_LINUXAIO
		3284	if (backend == EVBACKEND_LINUXAIO) linuxaio_destroy (EV_A);
2765	#endif	3285	#endif
2766	#if EV_USE_EPOLL	3286	#if EV_USE_EPOLL
2767	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);	3287	if (backend == EVBACKEND_EPOLL ) epoll_destroy (EV_A);
2768	#endif	3288	#endif
2769	#if EV_USE_POLL	3289	#if EV_USE_POLL
2770	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);	3290	if (backend == EVBACKEND_POLL ) poll_destroy (EV_A);
2771	#endif	3291	#endif
2772	#if EV_USE_SELECT	3292	#if EV_USE_SELECT
2773	if (backend == EVBACKEND_SELECT) select_destroy (EV_A);	3293	if (backend == EVBACKEND_SELECT ) select_destroy (EV_A);
2774	#endif	3294	#endif
2775		3295
2776	for (i = NUMPRI; i--; )	3296	for (i = NUMPRI; i--; )
2777	{	3297	{
2778	array_free (pending, [i]);	3298	array_free (pending, [i]);
…		…
2820		3340
2821	inline_size void	3341	inline_size void
2822	loop_fork (EV_P)	3342	loop_fork (EV_P)
2823	{	3343	{
2824	#if EV_USE_PORT	3344	#if EV_USE_PORT
2825	if (backend == EVBACKEND_PORT ) port_fork (EV_A);	3345	if (backend == EVBACKEND_PORT ) port_fork (EV_A);
2826	#endif	3346	#endif
2827	#if EV_USE_KQUEUE	3347	#if EV_USE_KQUEUE
2828	if (backend == EVBACKEND_KQUEUE) kqueue_fork (EV_A);	3348	if (backend == EVBACKEND_KQUEUE ) kqueue_fork (EV_A);
		3349	#endif
		3350	#if EV_USE_IOURING
		3351	if (backend == EVBACKEND_IOURING ) iouring_fork (EV_A);
		3352	#endif
		3353	#if EV_USE_LINUXAIO
		3354	if (backend == EVBACKEND_LINUXAIO) linuxaio_fork (EV_A);
2829	#endif	3355	#endif
2830	#if EV_USE_EPOLL	3356	#if EV_USE_EPOLL
2831	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);	3357	if (backend == EVBACKEND_EPOLL ) epoll_fork (EV_A);
2832	#endif	3358	#endif
2833	#if EV_USE_INOTIFY	3359	#if EV_USE_INOTIFY
2834	infy_fork (EV_A);	3360	infy_fork (EV_A);
2835	#endif	3361	#endif
2836		3362
		3363	if (postfork != 2)
		3364	{
		3365	#if EV_USE_SIGNALFD
		3366	/* surprisingly, nothing needs to be done for signalfd, accoridng to docs, it does the right thing on fork */
		3367	#endif
		3368
		3369	#if EV_USE_TIMERFD
		3370	if (ev_is_active (&timerfd_w))
		3371	{
		3372	ev_ref (EV_A);
		3373	ev_io_stop (EV_A_ &timerfd_w);
		3374
		3375	close (timerfd);
		3376	timerfd = -2;
		3377
		3378	evtimerfd_init (EV_A);
		3379	/* reschedule periodics, in case we missed something */
		3380	ev_feed_event (EV_A_ &timerfd_w, EV_CUSTOM);
		3381	}
		3382	#endif
		3383
2837	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE	3384	#if EV_SIGNAL_ENABLE || EV_ASYNC_ENABLE
2838	if (ev_is_active (&pipe_w))	3385	if (ev_is_active (&pipe_w))
2839	{	3386	{
2840	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */	3387	/* pipe_write_wanted must be false now, so modifying fd vars should be safe */
2841		3388
2842	ev_ref (EV_A);	3389	ev_ref (EV_A);
2843	ev_io_stop (EV_A_ &pipe_w);	3390	ev_io_stop (EV_A_ &pipe_w);
2844		3391
2845	if (evpipe [0] >= 0)	3392	if (evpipe [0] >= 0)
2846	EV_WIN32_CLOSE_FD (evpipe [0]);	3393	EV_WIN32_CLOSE_FD (evpipe [0]);
2847		3394
2848	evpipe_init (EV_A);	3395	evpipe_init (EV_A);
2849	/* iterate over everything, in case we missed something before */	3396	/* iterate over everything, in case we missed something before */
2850	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);	3397	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);
		3398	}
		3399	#endif
2851	}	3400	}
2852	#endif
2853		3401
2854	postfork = 0;	3402	postfork = 0;
2855	}	3403	}
2856		3404
2857	#if EV_MULTIPLICITY	3405	#if EV_MULTIPLICITY
2858		3406
		3407	ecb_cold
2859	struct ev_loop * ecb_cold	3408	struct ev_loop *
2860	ev_loop_new (unsigned int flags) EV_THROW	3409	ev_loop_new (unsigned int flags) EV_NOEXCEPT
2861	{	3410	{
2862	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));	3411	EV_P = (struct ev_loop *)ev_malloc (sizeof (struct ev_loop));
2863		3412
2864	memset (EV_A, 0, sizeof (struct ev_loop));	3413	memset (EV_A, 0, sizeof (struct ev_loop));
2865	loop_init (EV_A_ flags);	3414	loop_init (EV_A_ flags);
…		…
2872	}	3421	}
2873		3422
2874	#endif /* multiplicity */	3423	#endif /* multiplicity */
2875		3424
2876	#if EV_VERIFY	3425	#if EV_VERIFY
2877	static void noinline ecb_cold	3426	ecb_noinline ecb_cold
		3427	static void
2878	verify_watcher (EV_P_ W w)	3428	verify_watcher (EV_P_ W w)
2879	{	3429	{
2880	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));	3430	assert (("libev: watcher has invalid priority", ABSPRI (w) >= 0 && ABSPRI (w) < NUMPRI));
2881		3431
2882	if (w->pending)	3432	if (w->pending)
2883	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));	3433	assert (("libev: pending watcher not on pending queue", pendings [ABSPRI (w)][w->pending - 1].w == w));
2884	}	3434	}
2885		3435
2886	static void noinline ecb_cold	3436	ecb_noinline ecb_cold
		3437	static void
2887	verify_heap (EV_P_ ANHE *heap, int N)	3438	verify_heap (EV_P_ ANHE *heap, int N)
2888	{	3439	{
2889	int i;	3440	int i;
2890		3441
2891	for (i = HEAP0; i < N + HEAP0; ++i)	3442	for (i = HEAP0; i < N + HEAP0; ++i)
…		…
2896		3447
2897	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));	3448	verify_watcher (EV_A_ (W)ANHE_w (heap [i]));
2898	}	3449	}
2899	}	3450	}
2900		3451
2901	static void noinline ecb_cold	3452	ecb_noinline ecb_cold
		3453	static void
2902	array_verify (EV_P_ W *ws, int cnt)	3454	array_verify (EV_P_ W *ws, int cnt)
2903	{	3455	{
2904	while (cnt--)	3456	while (cnt--)
2905	{	3457	{
2906	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));	3458	assert (("libev: active index mismatch", ev_active (ws [cnt]) == cnt + 1));
…		…
2909	}	3461	}
2910	#endif	3462	#endif
2911		3463
2912	#if EV_FEATURE_API	3464	#if EV_FEATURE_API
2913	void ecb_cold	3465	void ecb_cold
2914	ev_verify (EV_P) EV_THROW	3466	ev_verify (EV_P) EV_NOEXCEPT
2915	{	3467	{
2916	#if EV_VERIFY	3468	#if EV_VERIFY
2917	int i;	3469	int i;
2918	WL w, w2;	3470	WL w, w2;
2919		3471
…		…
2995	#endif	3547	#endif
2996	}	3548	}
2997	#endif	3549	#endif
2998		3550
2999	#if EV_MULTIPLICITY	3551	#if EV_MULTIPLICITY
		3552	ecb_cold
3000	struct ev_loop * ecb_cold	3553	struct ev_loop *
3001	#else	3554	#else
3002	int	3555	int
3003	#endif	3556	#endif
3004	ev_default_loop (unsigned int flags) EV_THROW	3557	ev_default_loop (unsigned int flags) EV_NOEXCEPT
3005	{	3558	{
3006	if (!ev_default_loop_ptr)	3559	if (!ev_default_loop_ptr)
3007	{	3560	{
3008	#if EV_MULTIPLICITY	3561	#if EV_MULTIPLICITY
3009	EV_P = ev_default_loop_ptr = &default_loop_struct;	3562	EV_P = ev_default_loop_ptr = &default_loop_struct;
…		…
3028		3581
3029	return ev_default_loop_ptr;	3582	return ev_default_loop_ptr;
3030	}	3583	}
3031		3584
3032	void	3585	void
3033	ev_loop_fork (EV_P) EV_THROW	3586	ev_loop_fork (EV_P) EV_NOEXCEPT
3034	{	3587	{
3035	postfork = 1;	3588	postfork = 1;
3036	}	3589	}
3037		3590
3038	/*****************************************************************************/	3591	/*****************************************************************************/
…		…
3042	{	3595	{
3043	EV_CB_INVOKE ((W)w, revents);	3596	EV_CB_INVOKE ((W)w, revents);
3044	}	3597	}
3045		3598
3046	unsigned int	3599	unsigned int
3047	ev_pending_count (EV_P) EV_THROW	3600	ev_pending_count (EV_P) EV_NOEXCEPT
3048	{	3601	{
3049	int pri;	3602	int pri;
3050	unsigned int count = 0;	3603	unsigned int count = 0;
3051		3604
3052	for (pri = NUMPRI; pri--; )	3605	for (pri = NUMPRI; pri--; )
3053	count += pendingcnt [pri];	3606	count += pendingcnt [pri];
3054		3607
3055	return count;	3608	return count;
3056	}	3609	}
3057		3610
3058	void noinline	3611	ecb_noinline
		3612	void
3059	ev_invoke_pending (EV_P)	3613	ev_invoke_pending (EV_P)
3060	{	3614	{
3061	pendingpri = NUMPRI;	3615	pendingpri = NUMPRI;
3062		3616
3063	while (pendingpri) /* pendingpri possibly gets modified in the inner loop */	3617	do
3064	{	3618	{
3065	--pendingpri;	3619	--pendingpri;
3066		3620
		3621	/* pendingpri possibly gets modified in the inner loop */
3067	while (pendingcnt [pendingpri])	3622	while (pendingcnt [pendingpri])
3068	{	3623	{
3069	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];	3624	ANPENDING *p = pendings [pendingpri] + --pendingcnt [pendingpri];
3070		3625
3071	p->w->pending = 0;	3626	p->w->pending = 0;
3072	EV_CB_INVOKE (p->w, p->events);	3627	EV_CB_INVOKE (p->w, p->events);
3073	EV_FREQUENT_CHECK;	3628	EV_FREQUENT_CHECK;
3074	}	3629	}
3075	}	3630	}
		3631	while (pendingpri);
3076	}	3632	}
3077		3633
3078	#if EV_IDLE_ENABLE	3634	#if EV_IDLE_ENABLE
3079	/* make idle watchers pending. this handles the "call-idle */	3635	/* make idle watchers pending. this handles the "call-idle */
3080	/* only when higher priorities are idle" logic */	3636	/* only when higher priorities are idle" logic */
3081	inline_size void	3637	inline_size void
3082	idle_reify (EV_P)	3638	idle_reify (EV_P)
3083	{	3639	{
3084	if (expect_false (idleall))	3640	if (ecb_expect_false (idleall))
3085	{	3641	{
3086	int pri;	3642	int pri;
3087		3643
3088	for (pri = NUMPRI; pri--; )	3644	for (pri = NUMPRI; pri--; )
3089	{	3645	{
…		…
3119	{	3675	{
3120	ev_at (w) += w->repeat;	3676	ev_at (w) += w->repeat;
3121	if (ev_at (w) < mn_now)	3677	if (ev_at (w) < mn_now)
3122	ev_at (w) = mn_now;	3678	ev_at (w) = mn_now;
3123		3679
3124	assert (("libev: negative ev_timer repeat value found while processing timers", w->repeat > 0.));	3680	assert (("libev: negative ev_timer repeat value found while processing timers", w->repeat > EV_TS_CONST (0.)));
3125		3681
3126	ANHE_at_cache (timers [HEAP0]);	3682	ANHE_at_cache (timers [HEAP0]);
3127	downheap (timers, timercnt, HEAP0);	3683	downheap (timers, timercnt, HEAP0);
3128	}	3684	}
3129	else	3685	else
…		…
3138	}	3694	}
3139	}	3695	}
3140		3696
3141	#if EV_PERIODIC_ENABLE	3697	#if EV_PERIODIC_ENABLE
3142		3698
3143	static void noinline	3699	ecb_noinline
		3700	static void
3144	periodic_recalc (EV_P_ ev_periodic *w)	3701	periodic_recalc (EV_P_ ev_periodic *w)
3145	{	3702	{
3146	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;	3703	ev_tstamp interval = w->interval > MIN_INTERVAL ? w->interval : MIN_INTERVAL;
3147	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);	3704	ev_tstamp at = w->offset + interval * ev_floor ((ev_rt_now - w->offset) / interval);
3148		3705
…		…
3150	while (at <= ev_rt_now)	3707	while (at <= ev_rt_now)
3151	{	3708	{
3152	ev_tstamp nat = at + w->interval;	3709	ev_tstamp nat = at + w->interval;
3153		3710
3154	/* when resolution fails us, we use ev_rt_now */	3711	/* when resolution fails us, we use ev_rt_now */
3155	if (expect_false (nat == at))	3712	if (ecb_expect_false (nat == at))
3156	{	3713	{
3157	at = ev_rt_now;	3714	at = ev_rt_now;
3158	break;	3715	break;
3159	}	3716	}
3160		3717
…		…
3206	}	3763	}
3207	}	3764	}
3208		3765
3209	/* simply recalculate all periodics */	3766	/* simply recalculate all periodics */
3210	/* TODO: maybe ensure that at least one event happens when jumping forward? */	3767	/* TODO: maybe ensure that at least one event happens when jumping forward? */
3211	static void noinline ecb_cold	3768	ecb_noinline ecb_cold
		3769	static void
3212	periodics_reschedule (EV_P)	3770	periodics_reschedule (EV_P)
3213	{	3771	{
3214	int i;	3772	int i;
3215		3773
3216	/* adjust periodics after time jump */	3774	/* adjust periodics after time jump */
…		…
3229	reheap (periodics, periodiccnt);	3787	reheap (periodics, periodiccnt);
3230	}	3788	}
3231	#endif	3789	#endif
3232		3790
3233	/* adjust all timers by a given offset */	3791	/* adjust all timers by a given offset */
3234	static void noinline ecb_cold	3792	ecb_noinline ecb_cold
		3793	static void
3235	timers_reschedule (EV_P_ ev_tstamp adjust)	3794	timers_reschedule (EV_P_ ev_tstamp adjust)
3236	{	3795	{
3237	int i;	3796	int i;
3238		3797
3239	for (i = 0; i < timercnt; ++i)	3798	for (i = 0; i < timercnt; ++i)
…		…
3248	/* also detect if there was a timejump, and act accordingly */	3807	/* also detect if there was a timejump, and act accordingly */
3249	inline_speed void	3808	inline_speed void
3250	time_update (EV_P_ ev_tstamp max_block)	3809	time_update (EV_P_ ev_tstamp max_block)
3251	{	3810	{
3252	#if EV_USE_MONOTONIC	3811	#if EV_USE_MONOTONIC
3253	if (expect_true (have_monotonic))	3812	if (ecb_expect_true (have_monotonic))
3254	{	3813	{
3255	int i;	3814	int i;
3256	ev_tstamp odiff = rtmn_diff;	3815	ev_tstamp odiff = rtmn_diff;
3257		3816
3258	mn_now = get_clock ();	3817	mn_now = get_clock ();
3259		3818
3260	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */	3819	/* only fetch the realtime clock every 0.5*MIN_TIMEJUMP seconds */
3261	/* interpolate in the meantime */	3820	/* interpolate in the meantime */
3262	if (expect_true (mn_now - now_floor < MIN_TIMEJUMP * .5))	3821	if (ecb_expect_true (mn_now - now_floor < EV_TS_CONST (MIN_TIMEJUMP * .5)))
3263	{	3822	{
3264	ev_rt_now = rtmn_diff + mn_now;	3823	ev_rt_now = rtmn_diff + mn_now;
3265	return;	3824	return;
3266	}	3825	}
3267		3826
…		…
3281	ev_tstamp diff;	3840	ev_tstamp diff;
3282	rtmn_diff = ev_rt_now - mn_now;	3841	rtmn_diff = ev_rt_now - mn_now;
3283		3842
3284	diff = odiff - rtmn_diff;	3843	diff = odiff - rtmn_diff;
3285		3844
3286	if (expect_true ((diff < 0. ? -diff : diff) < MIN_TIMEJUMP))	3845	if (ecb_expect_true ((diff < EV_TS_CONST (0.) ? -diff : diff) < EV_TS_CONST (MIN_TIMEJUMP)))
3287	return; /* all is well */	3846	return; /* all is well */
3288		3847
3289	ev_rt_now = ev_time ();	3848	ev_rt_now = ev_time ();
3290	mn_now = get_clock ();	3849	mn_now = get_clock ();
3291	now_floor = mn_now;	3850	now_floor = mn_now;
…		…
3300	else	3859	else
3301	#endif	3860	#endif
3302	{	3861	{
3303	ev_rt_now = ev_time ();	3862	ev_rt_now = ev_time ();
3304		3863
3305	if (expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + MIN_TIMEJUMP))	3864	if (ecb_expect_false (mn_now > ev_rt_now || ev_rt_now > mn_now + max_block + EV_TS_CONST (MIN_TIMEJUMP)))
3306	{	3865	{
3307	/* adjust timers. this is easy, as the offset is the same for all of them */	3866	/* adjust timers. this is easy, as the offset is the same for all of them */
3308	timers_reschedule (EV_A_ ev_rt_now - mn_now);	3867	timers_reschedule (EV_A_ ev_rt_now - mn_now);
3309	#if EV_PERIODIC_ENABLE	3868	#if EV_PERIODIC_ENABLE
3310	periodics_reschedule (EV_A);	3869	periodics_reschedule (EV_A);
…		…
3333	#if EV_VERIFY >= 2	3892	#if EV_VERIFY >= 2
3334	ev_verify (EV_A);	3893	ev_verify (EV_A);
3335	#endif	3894	#endif
3336		3895
3337	#ifndef _WIN32	3896	#ifndef _WIN32
3338	if (expect_false (curpid)) /* penalise the forking check even more */	3897	if (ecb_expect_false (curpid)) /* penalise the forking check even more */
3339	if (expect_false (getpid () != curpid))	3898	if (ecb_expect_false (getpid () != curpid))
3340	{	3899	{
3341	curpid = getpid ();	3900	curpid = getpid ();
3342	postfork = 1;	3901	postfork = 1;
3343	}	3902	}
3344	#endif	3903	#endif
3345		3904
3346	#if EV_FORK_ENABLE	3905	#if EV_FORK_ENABLE
3347	/* we might have forked, so queue fork handlers */	3906	/* we might have forked, so queue fork handlers */
3348	if (expect_false (postfork))	3907	if (ecb_expect_false (postfork))
3349	if (forkcnt)	3908	if (forkcnt)
3350	{	3909	{
3351	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);	3910	queue_events (EV_A_ (W *)forks, forkcnt, EV_FORK);
3352	EV_INVOKE_PENDING;	3911	EV_INVOKE_PENDING;
3353	}	3912	}
3354	#endif	3913	#endif
3355		3914
3356	#if EV_PREPARE_ENABLE	3915	#if EV_PREPARE_ENABLE
3357	/* queue prepare watchers (and execute them) */	3916	/* queue prepare watchers (and execute them) */
3358	if (expect_false (preparecnt))	3917	if (ecb_expect_false (preparecnt))
3359	{	3918	{
3360	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);	3919	queue_events (EV_A_ (W *)prepares, preparecnt, EV_PREPARE);
3361	EV_INVOKE_PENDING;	3920	EV_INVOKE_PENDING;
3362	}	3921	}
3363	#endif	3922	#endif
3364		3923
3365	if (expect_false (loop_done))	3924	if (ecb_expect_false (loop_done))
3366	break;	3925	break;
3367		3926
3368	/* we might have forked, so reify kernel state if necessary */	3927	/* we might have forked, so reify kernel state if necessary */
3369	if (expect_false (postfork))	3928	if (ecb_expect_false (postfork))
3370	loop_fork (EV_A);	3929	loop_fork (EV_A);
3371		3930
3372	/* update fd-related kernel structures */	3931	/* update fd-related kernel structures */
3373	fd_reify (EV_A);	3932	fd_reify (EV_A);
3374		3933
…		…
3379		3938
3380	/* remember old timestamp for io_blocktime calculation */	3939	/* remember old timestamp for io_blocktime calculation */
3381	ev_tstamp prev_mn_now = mn_now;	3940	ev_tstamp prev_mn_now = mn_now;
3382		3941
3383	/* update time to cancel out callback processing overhead */	3942	/* update time to cancel out callback processing overhead */
3384	time_update (EV_A_ 1e100);	3943	time_update (EV_A_ EV_TS_CONST (EV_TSTAMP_HUGE));
3385		3944
3386	/* from now on, we want a pipe-wake-up */	3945	/* from now on, we want a pipe-wake-up */
3387	pipe_write_wanted = 1;	3946	pipe_write_wanted = 1;
3388		3947
3389	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */	3948	ECB_MEMORY_FENCE; /* make sure pipe_write_wanted is visible before we check for potential skips */
3390		3949
3391	if (expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))	3950	if (ecb_expect_true (!(flags & EVRUN_NOWAIT || idleall || !activecnt || pipe_write_skipped)))
3392	{	3951	{
3393	waittime = MAX_BLOCKTIME;	3952	waittime = EV_TS_CONST (MAX_BLOCKTIME);
3394		3953
3395	if (timercnt)	3954	if (timercnt)
3396	{	3955	{
3397	ev_tstamp to = ANHE_at (timers [HEAP0]) - mn_now;	3956	ev_tstamp to = ANHE_at (timers [HEAP0]) - mn_now;
3398	if (waittime > to) waittime = to;	3957	if (waittime > to) waittime = to;
…		…
3405	if (waittime > to) waittime = to;	3964	if (waittime > to) waittime = to;
3406	}	3965	}
3407	#endif	3966	#endif
3408		3967
3409	/* don't let timeouts decrease the waittime below timeout_blocktime */	3968	/* don't let timeouts decrease the waittime below timeout_blocktime */
3410	if (expect_false (waittime < timeout_blocktime))	3969	if (ecb_expect_false (waittime < timeout_blocktime))
3411	waittime = timeout_blocktime;	3970	waittime = timeout_blocktime;
3412		3971
3413	/* at this point, we NEED to wait, so we have to ensure */	3972	/* now there are two more special cases left, either we have
3414	/* to pass a minimum nonzero value to the backend */	3973	* already-expired timers, so we should not sleep, or we have timers
		3974	* that expire very soon, in which case we need to wait for a minimum
		3975	* amount of time for some event loop backends.
		3976	*/
3415	if (expect_false (waittime < backend_mintime))	3977	if (ecb_expect_false (waittime < backend_mintime))
		3978	waittime = waittime <= EV_TS_CONST (0.)
		3979	? EV_TS_CONST (0.)
3416	waittime = backend_mintime;	3980	: backend_mintime;
3417		3981
3418	/* extra check because io_blocktime is commonly 0 */	3982	/* extra check because io_blocktime is commonly 0 */
3419	if (expect_false (io_blocktime))	3983	if (ecb_expect_false (io_blocktime))
3420	{	3984	{
3421	sleeptime = io_blocktime - (mn_now - prev_mn_now);	3985	sleeptime = io_blocktime - (mn_now - prev_mn_now);
3422		3986
3423	if (sleeptime > waittime - backend_mintime)	3987	if (sleeptime > waittime - backend_mintime)
3424	sleeptime = waittime - backend_mintime;	3988	sleeptime = waittime - backend_mintime;
3425		3989
3426	if (expect_true (sleeptime > 0.))	3990	if (ecb_expect_true (sleeptime > EV_TS_CONST (0.)))
3427	{	3991	{
3428	ev_sleep (sleeptime);	3992	ev_sleep (sleeptime);
3429	waittime -= sleeptime;	3993	waittime -= sleeptime;
3430	}	3994	}
3431	}	3995	}
…		…
3445	{	4009	{
3446	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));	4010	assert (("libev: pipe_w not active, but pipe not written", ev_is_active (&pipe_w)));
3447	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);	4011	ev_feed_event (EV_A_ &pipe_w, EV_CUSTOM);
3448	}	4012	}
3449		4013
3450
3451	/* update ev_rt_now, do magic */	4014	/* update ev_rt_now, do magic */
3452	time_update (EV_A_ waittime + sleeptime);	4015	time_update (EV_A_ waittime + sleeptime);
3453	}	4016	}
3454		4017
3455	/* queue pending timers and reschedule them */	4018	/* queue pending timers and reschedule them */
…		…
3463	idle_reify (EV_A);	4026	idle_reify (EV_A);
3464	#endif	4027	#endif
3465		4028
3466	#if EV_CHECK_ENABLE	4029	#if EV_CHECK_ENABLE
3467	/* queue check watchers, to be executed first */	4030	/* queue check watchers, to be executed first */
3468	if (expect_false (checkcnt))	4031	if (ecb_expect_false (checkcnt))
3469	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);	4032	queue_events (EV_A_ (W *)checks, checkcnt, EV_CHECK);
3470	#endif	4033	#endif
3471		4034
3472	EV_INVOKE_PENDING;	4035	EV_INVOKE_PENDING;
3473	}	4036	}
3474	while (expect_true (	4037	while (ecb_expect_true (
3475	activecnt	4038	activecnt
3476	&& !loop_done	4039	&& !loop_done
3477	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))	4040	&& !(flags & (EVRUN_ONCE | EVRUN_NOWAIT))
3478	));	4041	));
3479		4042
…		…
3486		4049
3487	return activecnt;	4050	return activecnt;
3488	}	4051	}
3489		4052
3490	void	4053	void
3491	ev_break (EV_P_ int how) EV_THROW	4054	ev_break (EV_P_ int how) EV_NOEXCEPT
3492	{	4055	{
3493	loop_done = how;	4056	loop_done = how;
3494	}	4057	}
3495		4058
3496	void	4059	void
3497	ev_ref (EV_P) EV_THROW	4060	ev_ref (EV_P) EV_NOEXCEPT
3498	{	4061	{
3499	++activecnt;	4062	++activecnt;
3500	}	4063	}
3501		4064
3502	void	4065	void
3503	ev_unref (EV_P) EV_THROW	4066	ev_unref (EV_P) EV_NOEXCEPT
3504	{	4067	{
3505	--activecnt;	4068	--activecnt;
3506	}	4069	}
3507		4070
3508	void	4071	void
3509	ev_now_update (EV_P) EV_THROW	4072	ev_now_update (EV_P) EV_NOEXCEPT
3510	{	4073	{
3511	time_update (EV_A_ 1e100);	4074	time_update (EV_A_ EV_TSTAMP_HUGE);
3512	}	4075	}
3513		4076
3514	void	4077	void
3515	ev_suspend (EV_P) EV_THROW	4078	ev_suspend (EV_P) EV_NOEXCEPT
3516	{	4079	{
3517	ev_now_update (EV_A);	4080	ev_now_update (EV_A);
3518	}	4081	}
3519		4082
3520	void	4083	void
3521	ev_resume (EV_P) EV_THROW	4084	ev_resume (EV_P) EV_NOEXCEPT
3522	{	4085	{
3523	ev_tstamp mn_prev = mn_now;	4086	ev_tstamp mn_prev = mn_now;
3524		4087
3525	ev_now_update (EV_A);	4088	ev_now_update (EV_A);
3526	timers_reschedule (EV_A_ mn_now - mn_prev);	4089	timers_reschedule (EV_A_ mn_now - mn_prev);
…		…
3543	inline_size void	4106	inline_size void
3544	wlist_del (WL *head, WL elem)	4107	wlist_del (WL *head, WL elem)
3545	{	4108	{
3546	while (*head)	4109	while (*head)
3547	{	4110	{
3548	if (expect_true (*head == elem))	4111	if (ecb_expect_true (*head == elem))
3549	{	4112	{
3550	*head = elem->next;	4113	*head = elem->next;
3551	break;	4114	break;
3552	}	4115	}
3553		4116
…		…
3565	w->pending = 0;	4128	w->pending = 0;
3566	}	4129	}
3567	}	4130	}
3568		4131
3569	int	4132	int
3570	ev_clear_pending (EV_P_ void *w) EV_THROW	4133	ev_clear_pending (EV_P_ void *w) EV_NOEXCEPT
3571	{	4134	{
3572	W w_ = (W)w;	4135	W w_ = (W)w;
3573	int pending = w_->pending;	4136	int pending = w_->pending;
3574		4137
3575	if (expect_true (pending))	4138	if (ecb_expect_true (pending))
3576	{	4139	{
3577	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;	4140	ANPENDING *p = pendings [ABSPRI (w_)] + pending - 1;
3578	p->w = (W)&pending_w;	4141	p->w = (W)&pending_w;
3579	w_->pending = 0;	4142	w_->pending = 0;
3580	return p->events;	4143	return p->events;
…		…
3607	w->active = 0;	4170	w->active = 0;
3608	}	4171	}
3609		4172
3610	/*****************************************************************************/	4173	/*****************************************************************************/
3611		4174
3612	void noinline	4175	ecb_noinline
		4176	void
3613	ev_io_start (EV_P_ ev_io *w) EV_THROW	4177	ev_io_start (EV_P_ ev_io *w) EV_NOEXCEPT
3614	{	4178	{
3615	int fd = w->fd;	4179	int fd = w->fd;
3616		4180
3617	if (expect_false (ev_is_active (w)))	4181	if (ecb_expect_false (ev_is_active (w)))
3618	return;	4182	return;
3619		4183
3620	assert (("libev: ev_io_start called with negative fd", fd >= 0));	4184	assert (("libev: ev_io_start called with negative fd", fd >= 0));
3621	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));	4185	assert (("libev: ev_io_start called with illegal event mask", !(w->events & ~(EV__IOFDSET | EV_READ | EV_WRITE))));
3622		4186
		4187	#if EV_VERIFY >= 2
		4188	assert (("libev: ev_io_start called on watcher with invalid fd", fd_valid (fd)));
		4189	#endif
3623	EV_FREQUENT_CHECK;	4190	EV_FREQUENT_CHECK;
3624		4191
3625	ev_start (EV_A_ (W)w, 1);	4192	ev_start (EV_A_ (W)w, 1);
3626	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_init_zero);	4193	array_needsize (ANFD, anfds, anfdmax, fd + 1, array_needsize_zerofill);
3627	wlist_add (&anfds[fd].head, (WL)w);	4194	wlist_add (&anfds[fd].head, (WL)w);
3628		4195
3629	/* common bug, apparently */	4196	/* common bug, apparently */
3630	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));	4197	assert (("libev: ev_io_start called with corrupted watcher", ((WL)w)->next != (WL)w));
3631		4198
…		…
3633	w->events &= ~EV__IOFDSET;	4200	w->events &= ~EV__IOFDSET;
3634		4201
3635	EV_FREQUENT_CHECK;	4202	EV_FREQUENT_CHECK;
3636	}	4203	}
3637		4204
3638	void noinline	4205	ecb_noinline
		4206	void
3639	ev_io_stop (EV_P_ ev_io *w) EV_THROW	4207	ev_io_stop (EV_P_ ev_io *w) EV_NOEXCEPT
3640	{	4208	{
3641	clear_pending (EV_A_ (W)w);	4209	clear_pending (EV_A_ (W)w);
3642	if (expect_false (!ev_is_active (w)))	4210	if (ecb_expect_false (!ev_is_active (w)))
3643	return;	4211	return;
3644		4212
3645	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));	4213	assert (("libev: ev_io_stop called with illegal fd (must stay constant after start!)", w->fd >= 0 && w->fd < anfdmax));
3646		4214
		4215	#if EV_VERIFY >= 2
		4216	assert (("libev: ev_io_stop called on watcher with invalid fd", fd_valid (w->fd)));
		4217	#endif
3647	EV_FREQUENT_CHECK;	4218	EV_FREQUENT_CHECK;
3648		4219
3649	wlist_del (&anfds[w->fd].head, (WL)w);	4220	wlist_del (&anfds[w->fd].head, (WL)w);
3650	ev_stop (EV_A_ (W)w);	4221	ev_stop (EV_A_ (W)w);
3651		4222
3652	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);	4223	fd_change (EV_A_ w->fd, EV_ANFD_REIFY);
3653		4224
3654	EV_FREQUENT_CHECK;	4225	EV_FREQUENT_CHECK;
3655	}	4226	}
3656		4227
3657	void noinline	4228	ecb_noinline
		4229	void
3658	ev_timer_start (EV_P_ ev_timer *w) EV_THROW	4230	ev_timer_start (EV_P_ ev_timer *w) EV_NOEXCEPT
3659	{	4231	{
3660	if (expect_false (ev_is_active (w)))	4232	if (ecb_expect_false (ev_is_active (w)))
3661	return;	4233	return;
3662		4234
3663	ev_at (w) += mn_now;	4235	ev_at (w) += mn_now;
3664		4236
3665	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));	4237	assert (("libev: ev_timer_start called with negative timer repeat value", w->repeat >= 0.));
3666		4238
3667	EV_FREQUENT_CHECK;	4239	EV_FREQUENT_CHECK;
3668		4240
3669	++timercnt;	4241	++timercnt;
3670	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);	4242	ev_start (EV_A_ (W)w, timercnt + HEAP0 - 1);
3671	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, EMPTY2);	4243	array_needsize (ANHE, timers, timermax, ev_active (w) + 1, array_needsize_noinit);
3672	ANHE_w (timers [ev_active (w)]) = (WT)w;	4244	ANHE_w (timers [ev_active (w)]) = (WT)w;
3673	ANHE_at_cache (timers [ev_active (w)]);	4245	ANHE_at_cache (timers [ev_active (w)]);
3674	upheap (timers, ev_active (w));	4246	upheap (timers, ev_active (w));
3675		4247
3676	EV_FREQUENT_CHECK;	4248	EV_FREQUENT_CHECK;
3677		4249
3678	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/	4250	/*assert (("libev: internal timer heap corruption", timers [ev_active (w)] == (WT)w));*/
3679	}	4251	}
3680		4252
3681	void noinline	4253	ecb_noinline
		4254	void
3682	ev_timer_stop (EV_P_ ev_timer *w) EV_THROW	4255	ev_timer_stop (EV_P_ ev_timer *w) EV_NOEXCEPT
3683	{	4256	{
3684	clear_pending (EV_A_ (W)w);	4257	clear_pending (EV_A_ (W)w);
3685	if (expect_false (!ev_is_active (w)))	4258	if (ecb_expect_false (!ev_is_active (w)))
3686	return;	4259	return;
3687		4260
3688	EV_FREQUENT_CHECK;	4261	EV_FREQUENT_CHECK;
3689		4262
3690	{	4263	{
…		…
3692		4265
3693	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));	4266	assert (("libev: internal timer heap corruption", ANHE_w (timers [active]) == (WT)w));
3694		4267
3695	--timercnt;	4268	--timercnt;
3696		4269
3697	if (expect_true (active < timercnt + HEAP0))	4270	if (ecb_expect_true (active < timercnt + HEAP0))
3698	{	4271	{
3699	timers [active] = timers [timercnt + HEAP0];	4272	timers [active] = timers [timercnt + HEAP0];
3700	adjustheap (timers, timercnt, active);	4273	adjustheap (timers, timercnt, active);
3701	}	4274	}
3702	}	4275	}
…		…
3706	ev_stop (EV_A_ (W)w);	4279	ev_stop (EV_A_ (W)w);
3707		4280
3708	EV_FREQUENT_CHECK;	4281	EV_FREQUENT_CHECK;
3709	}	4282	}
3710		4283
3711	void noinline	4284	ecb_noinline
		4285	void
3712	ev_timer_again (EV_P_ ev_timer *w) EV_THROW	4286	ev_timer_again (EV_P_ ev_timer *w) EV_NOEXCEPT
3713	{	4287	{
3714	EV_FREQUENT_CHECK;	4288	EV_FREQUENT_CHECK;
3715		4289
3716	clear_pending (EV_A_ (W)w);	4290	clear_pending (EV_A_ (W)w);
3717		4291
…		…
3734		4308
3735	EV_FREQUENT_CHECK;	4309	EV_FREQUENT_CHECK;
3736	}	4310	}
3737		4311
3738	ev_tstamp	4312	ev_tstamp
3739	ev_timer_remaining (EV_P_ ev_timer *w) EV_THROW	4313	ev_timer_remaining (EV_P_ ev_timer *w) EV_NOEXCEPT
3740	{	4314	{
3741	return ev_at (w) - (ev_is_active (w) ? mn_now : 0.);	4315	return ev_at (w) - (ev_is_active (w) ? mn_now : EV_TS_CONST (0.));
3742	}	4316	}
3743		4317
3744	#if EV_PERIODIC_ENABLE	4318	#if EV_PERIODIC_ENABLE
3745	void noinline	4319	ecb_noinline
		4320	void
3746	ev_periodic_start (EV_P_ ev_periodic *w) EV_THROW	4321	ev_periodic_start (EV_P_ ev_periodic *w) EV_NOEXCEPT
3747	{	4322	{
3748	if (expect_false (ev_is_active (w)))	4323	if (ecb_expect_false (ev_is_active (w)))
3749	return;	4324	return;
		4325
		4326	#if EV_USE_TIMERFD
		4327	if (timerfd == -2)
		4328	evtimerfd_init (EV_A);
		4329	#endif
3750		4330
3751	if (w->reschedule_cb)	4331	if (w->reschedule_cb)
3752	ev_at (w) = w->reschedule_cb (w, ev_rt_now);	4332	ev_at (w) = w->reschedule_cb (w, ev_rt_now);
3753	else if (w->interval)	4333	else if (w->interval)
3754	{	4334	{
…		…
3760		4340
3761	EV_FREQUENT_CHECK;	4341	EV_FREQUENT_CHECK;
3762		4342
3763	++periodiccnt;	4343	++periodiccnt;
3764	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);	4344	ev_start (EV_A_ (W)w, periodiccnt + HEAP0 - 1);
3765	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, EMPTY2);	4345	array_needsize (ANHE, periodics, periodicmax, ev_active (w) + 1, array_needsize_noinit);
3766	ANHE_w (periodics [ev_active (w)]) = (WT)w;	4346	ANHE_w (periodics [ev_active (w)]) = (WT)w;
3767	ANHE_at_cache (periodics [ev_active (w)]);	4347	ANHE_at_cache (periodics [ev_active (w)]);
3768	upheap (periodics, ev_active (w));	4348	upheap (periodics, ev_active (w));
3769		4349
3770	EV_FREQUENT_CHECK;	4350	EV_FREQUENT_CHECK;
3771		4351
3772	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/	4352	/*assert (("libev: internal periodic heap corruption", ANHE_w (periodics [ev_active (w)]) == (WT)w));*/
3773	}	4353	}
3774		4354
3775	void noinline	4355	ecb_noinline
		4356	void
3776	ev_periodic_stop (EV_P_ ev_periodic *w) EV_THROW	4357	ev_periodic_stop (EV_P_ ev_periodic *w) EV_NOEXCEPT
3777	{	4358	{
3778	clear_pending (EV_A_ (W)w);	4359	clear_pending (EV_A_ (W)w);
3779	if (expect_false (!ev_is_active (w)))	4360	if (ecb_expect_false (!ev_is_active (w)))
3780	return;	4361	return;
3781		4362
3782	EV_FREQUENT_CHECK;	4363	EV_FREQUENT_CHECK;
3783		4364
3784	{	4365	{
…		…
3786		4367
3787	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));	4368	assert (("libev: internal periodic heap corruption", ANHE_w (periodics [active]) == (WT)w));
3788		4369
3789	--periodiccnt;	4370	--periodiccnt;
3790		4371
3791	if (expect_true (active < periodiccnt + HEAP0))	4372	if (ecb_expect_true (active < periodiccnt + HEAP0))
3792	{	4373	{
3793	periodics [active] = periodics [periodiccnt + HEAP0];	4374	periodics [active] = periodics [periodiccnt + HEAP0];
3794	adjustheap (periodics, periodiccnt, active);	4375	adjustheap (periodics, periodiccnt, active);
3795	}	4376	}
3796	}	4377	}
…		…
3798	ev_stop (EV_A_ (W)w);	4379	ev_stop (EV_A_ (W)w);
3799		4380
3800	EV_FREQUENT_CHECK;	4381	EV_FREQUENT_CHECK;
3801	}	4382	}
3802		4383
3803	void noinline	4384	ecb_noinline
		4385	void
3804	ev_periodic_again (EV_P_ ev_periodic *w) EV_THROW	4386	ev_periodic_again (EV_P_ ev_periodic *w) EV_NOEXCEPT
3805	{	4387	{
3806	/* TODO: use adjustheap and recalculation */	4388	/* TODO: use adjustheap and recalculation */
3807	ev_periodic_stop (EV_A_ w);	4389	ev_periodic_stop (EV_A_ w);
3808	ev_periodic_start (EV_A_ w);	4390	ev_periodic_start (EV_A_ w);
3809	}	4391	}
…		…
3813	# define SA_RESTART 0	4395	# define SA_RESTART 0
3814	#endif	4396	#endif
3815		4397
3816	#if EV_SIGNAL_ENABLE	4398	#if EV_SIGNAL_ENABLE
3817		4399
3818	void noinline	4400	ecb_noinline
		4401	void
3819	ev_signal_start (EV_P_ ev_signal *w) EV_THROW	4402	ev_signal_start (EV_P_ ev_signal *w) EV_NOEXCEPT
3820	{	4403	{
3821	if (expect_false (ev_is_active (w)))	4404	if (ecb_expect_false (ev_is_active (w)))
3822	return;	4405	return;
3823		4406
3824	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));	4407	assert (("libev: ev_signal_start called with illegal signal number", w->signum > 0 && w->signum < EV_NSIG));
3825		4408
3826	#if EV_MULTIPLICITY	4409	#if EV_MULTIPLICITY
…		…
3895	}	4478	}
3896		4479
3897	EV_FREQUENT_CHECK;	4480	EV_FREQUENT_CHECK;
3898	}	4481	}
3899		4482
3900	void noinline	4483	ecb_noinline
		4484	void
3901	ev_signal_stop (EV_P_ ev_signal *w) EV_THROW	4485	ev_signal_stop (EV_P_ ev_signal *w) EV_NOEXCEPT
3902	{	4486	{
3903	clear_pending (EV_A_ (W)w);	4487	clear_pending (EV_A_ (W)w);
3904	if (expect_false (!ev_is_active (w)))	4488	if (ecb_expect_false (!ev_is_active (w)))
3905	return;	4489	return;
3906		4490
3907	EV_FREQUENT_CHECK;	4491	EV_FREQUENT_CHECK;
3908		4492
3909	wlist_del (&signals [w->signum - 1].head, (WL)w);	4493	wlist_del (&signals [w->signum - 1].head, (WL)w);
…		…
3937	#endif	4521	#endif
3938		4522
3939	#if EV_CHILD_ENABLE	4523	#if EV_CHILD_ENABLE
3940		4524
3941	void	4525	void
3942	ev_child_start (EV_P_ ev_child *w) EV_THROW	4526	ev_child_start (EV_P_ ev_child *w) EV_NOEXCEPT
3943	{	4527	{
3944	#if EV_MULTIPLICITY	4528	#if EV_MULTIPLICITY
3945	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));	4529	assert (("libev: child watchers are only supported in the default loop", loop == ev_default_loop_ptr));
3946	#endif	4530	#endif
3947	if (expect_false (ev_is_active (w)))	4531	if (ecb_expect_false (ev_is_active (w)))
3948	return;	4532	return;
3949		4533
3950	EV_FREQUENT_CHECK;	4534	EV_FREQUENT_CHECK;
3951		4535
3952	ev_start (EV_A_ (W)w, 1);	4536	ev_start (EV_A_ (W)w, 1);
…		…
3954		4538
3955	EV_FREQUENT_CHECK;	4539	EV_FREQUENT_CHECK;
3956	}	4540	}
3957		4541
3958	void	4542	void
3959	ev_child_stop (EV_P_ ev_child *w) EV_THROW	4543	ev_child_stop (EV_P_ ev_child *w) EV_NOEXCEPT
3960	{	4544	{
3961	clear_pending (EV_A_ (W)w);	4545	clear_pending (EV_A_ (W)w);
3962	if (expect_false (!ev_is_active (w)))	4546	if (ecb_expect_false (!ev_is_active (w)))
3963	return;	4547	return;
3964		4548
3965	EV_FREQUENT_CHECK;	4549	EV_FREQUENT_CHECK;
3966		4550
3967	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);	4551	wlist_del (&childs [w->pid & ((EV_PID_HASHSIZE) - 1)], (WL)w);
…		…
3981		4565
3982	#define DEF_STAT_INTERVAL 5.0074891	4566	#define DEF_STAT_INTERVAL 5.0074891
3983	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */	4567	#define NFS_STAT_INTERVAL 30.1074891 /* for filesystems potentially failing inotify */
3984	#define MIN_STAT_INTERVAL 0.1074891	4568	#define MIN_STAT_INTERVAL 0.1074891
3985		4569
3986	static void noinline stat_timer_cb (EV_P_ ev_timer *w_, int revents);	4570	ecb_noinline static void stat_timer_cb (EV_P_ ev_timer *w_, int revents);
3987		4571
3988	#if EV_USE_INOTIFY	4572	#if EV_USE_INOTIFY
3989		4573
3990	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */	4574	/* the * 2 is to allow for alignment padding, which for some reason is >> 8 */
3991	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)	4575	# define EV_INOTIFY_BUFSIZE (sizeof (struct inotify_event) * 2 + NAME_MAX)
3992		4576
3993	static void noinline	4577	ecb_noinline
		4578	static void
3994	infy_add (EV_P_ ev_stat *w)	4579	infy_add (EV_P_ ev_stat *w)
3995	{	4580	{
3996	w->wd = inotify_add_watch (fs_fd, w->path,	4581	w->wd = inotify_add_watch (fs_fd, w->path,
3997	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY	4582	IN_ATTRIB | IN_DELETE_SELF | IN_MOVE_SELF | IN_MODIFY
3998	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO	4583	| IN_CREATE | IN_DELETE | IN_MOVED_FROM | IN_MOVED_TO
…		…
4062	if (ev_is_active (&w->timer)) ev_ref (EV_A);	4647	if (ev_is_active (&w->timer)) ev_ref (EV_A);
4063	ev_timer_again (EV_A_ &w->timer);	4648	ev_timer_again (EV_A_ &w->timer);
4064	if (ev_is_active (&w->timer)) ev_unref (EV_A);	4649	if (ev_is_active (&w->timer)) ev_unref (EV_A);
4065	}	4650	}
4066		4651
4067	static void noinline	4652	ecb_noinline
		4653	static void
4068	infy_del (EV_P_ ev_stat *w)	4654	infy_del (EV_P_ ev_stat *w)
4069	{	4655	{
4070	int slot;	4656	int slot;
4071	int wd = w->wd;	4657	int wd = w->wd;
4072		4658
…		…
4079		4665
4080	/* remove this watcher, if others are watching it, they will rearm */	4666	/* remove this watcher, if others are watching it, they will rearm */
4081	inotify_rm_watch (fs_fd, wd);	4667	inotify_rm_watch (fs_fd, wd);
4082	}	4668	}
4083		4669
4084	static void noinline	4670	ecb_noinline
		4671	static void
4085	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)	4672	infy_wd (EV_P_ int slot, int wd, struct inotify_event *ev)
4086	{	4673	{
4087	if (slot < 0)	4674	if (slot < 0)
4088	/* overflow, need to check for all hash slots */	4675	/* overflow, need to check for all hash slots */
4089	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)	4676	for (slot = 0; slot < (EV_INOTIFY_HASHSIZE); ++slot)
…		…
4125	infy_wd (EV_A_ ev->wd, ev->wd, ev);	4712	infy_wd (EV_A_ ev->wd, ev->wd, ev);
4126	ofs += sizeof (struct inotify_event) + ev->len;	4713	ofs += sizeof (struct inotify_event) + ev->len;
4127	}	4714	}
4128	}	4715	}
4129		4716
4130	inline_size void ecb_cold	4717	inline_size ecb_cold
		4718	void
4131	ev_check_2625 (EV_P)	4719	ev_check_2625 (EV_P)
4132	{	4720	{
4133	/* kernels < 2.6.25 are borked	4721	/* kernels < 2.6.25 are borked
4134	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html	4722	* http://www.ussg.indiana.edu/hypermail/linux/kernel/0711.3/1208.html
4135	*/	4723	*/
…		…
4225	#else	4813	#else
4226	# define EV_LSTAT(p,b) lstat (p, b)	4814	# define EV_LSTAT(p,b) lstat (p, b)
4227	#endif	4815	#endif
4228		4816
4229	void	4817	void
4230	ev_stat_stat (EV_P_ ev_stat *w) EV_THROW	4818	ev_stat_stat (EV_P_ ev_stat *w) EV_NOEXCEPT
4231	{	4819	{
4232	if (lstat (w->path, &w->attr) < 0)	4820	if (lstat (w->path, &w->attr) < 0)
4233	w->attr.st_nlink = 0;	4821	w->attr.st_nlink = 0;
4234	else if (!w->attr.st_nlink)	4822	else if (!w->attr.st_nlink)
4235	w->attr.st_nlink = 1;	4823	w->attr.st_nlink = 1;
4236	}	4824	}
4237		4825
4238	static void noinline	4826	ecb_noinline
		4827	static void
4239	stat_timer_cb (EV_P_ ev_timer *w_, int revents)	4828	stat_timer_cb (EV_P_ ev_timer *w_, int revents)
4240	{	4829	{
4241	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));	4830	ev_stat *w = (ev_stat *)(((char *)w_) - offsetof (ev_stat, timer));
4242		4831
4243	ev_statdata prev = w->attr;	4832	ev_statdata prev = w->attr;
…		…
4274	ev_feed_event (EV_A_ w, EV_STAT);	4863	ev_feed_event (EV_A_ w, EV_STAT);
4275	}	4864	}
4276	}	4865	}
4277		4866
4278	void	4867	void
4279	ev_stat_start (EV_P_ ev_stat *w) EV_THROW	4868	ev_stat_start (EV_P_ ev_stat *w) EV_NOEXCEPT
4280	{	4869	{
4281	if (expect_false (ev_is_active (w)))	4870	if (ecb_expect_false (ev_is_active (w)))
4282	return;	4871	return;
4283		4872
4284	ev_stat_stat (EV_A_ w);	4873	ev_stat_stat (EV_A_ w);
4285		4874
4286	if (w->interval < MIN_STAT_INTERVAL && w->interval)	4875	if (w->interval < MIN_STAT_INTERVAL && w->interval)
…		…
4305		4894
4306	EV_FREQUENT_CHECK;	4895	EV_FREQUENT_CHECK;
4307	}	4896	}
4308		4897
4309	void	4898	void
4310	ev_stat_stop (EV_P_ ev_stat *w) EV_THROW	4899	ev_stat_stop (EV_P_ ev_stat *w) EV_NOEXCEPT
4311	{	4900	{
4312	clear_pending (EV_A_ (W)w);	4901	clear_pending (EV_A_ (W)w);
4313	if (expect_false (!ev_is_active (w)))	4902	if (ecb_expect_false (!ev_is_active (w)))
4314	return;	4903	return;
4315		4904
4316	EV_FREQUENT_CHECK;	4905	EV_FREQUENT_CHECK;
4317		4906
4318	#if EV_USE_INOTIFY	4907	#if EV_USE_INOTIFY
…		…
4331	}	4920	}
4332	#endif	4921	#endif
4333		4922
4334	#if EV_IDLE_ENABLE	4923	#if EV_IDLE_ENABLE
4335	void	4924	void
4336	ev_idle_start (EV_P_ ev_idle *w) EV_THROW	4925	ev_idle_start (EV_P_ ev_idle *w) EV_NOEXCEPT
4337	{	4926	{
4338	if (expect_false (ev_is_active (w)))	4927	if (ecb_expect_false (ev_is_active (w)))
4339	return;	4928	return;
4340		4929
4341	pri_adjust (EV_A_ (W)w);	4930	pri_adjust (EV_A_ (W)w);
4342		4931
4343	EV_FREQUENT_CHECK;	4932	EV_FREQUENT_CHECK;
…		…
4346	int active = ++idlecnt [ABSPRI (w)];	4935	int active = ++idlecnt [ABSPRI (w)];
4347		4936
4348	++idleall;	4937	++idleall;
4349	ev_start (EV_A_ (W)w, active);	4938	ev_start (EV_A_ (W)w, active);
4350		4939
4351	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, EMPTY2);	4940	array_needsize (ev_idle *, idles [ABSPRI (w)], idlemax [ABSPRI (w)], active, array_needsize_noinit);
4352	idles [ABSPRI (w)][active - 1] = w;	4941	idles [ABSPRI (w)][active - 1] = w;
4353	}	4942	}
4354		4943
4355	EV_FREQUENT_CHECK;	4944	EV_FREQUENT_CHECK;
4356	}	4945	}
4357		4946
4358	void	4947	void
4359	ev_idle_stop (EV_P_ ev_idle *w) EV_THROW	4948	ev_idle_stop (EV_P_ ev_idle *w) EV_NOEXCEPT
4360	{	4949	{
4361	clear_pending (EV_A_ (W)w);	4950	clear_pending (EV_A_ (W)w);
4362	if (expect_false (!ev_is_active (w)))	4951	if (ecb_expect_false (!ev_is_active (w)))
4363	return;	4952	return;
4364		4953
4365	EV_FREQUENT_CHECK;	4954	EV_FREQUENT_CHECK;
4366		4955
4367	{	4956	{
…		…
4378	}	4967	}
4379	#endif	4968	#endif
4380		4969
4381	#if EV_PREPARE_ENABLE	4970	#if EV_PREPARE_ENABLE
4382	void	4971	void
4383	ev_prepare_start (EV_P_ ev_prepare *w) EV_THROW	4972	ev_prepare_start (EV_P_ ev_prepare *w) EV_NOEXCEPT
4384	{	4973	{
4385	if (expect_false (ev_is_active (w)))	4974	if (ecb_expect_false (ev_is_active (w)))
4386	return;	4975	return;
4387		4976
4388	EV_FREQUENT_CHECK;	4977	EV_FREQUENT_CHECK;
4389		4978
4390	ev_start (EV_A_ (W)w, ++preparecnt);	4979	ev_start (EV_A_ (W)w, ++preparecnt);
4391	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, EMPTY2);	4980	array_needsize (ev_prepare *, prepares, preparemax, preparecnt, array_needsize_noinit);
4392	prepares [preparecnt - 1] = w;	4981	prepares [preparecnt - 1] = w;
4393		4982
4394	EV_FREQUENT_CHECK;	4983	EV_FREQUENT_CHECK;
4395	}	4984	}
4396		4985
4397	void	4986	void
4398	ev_prepare_stop (EV_P_ ev_prepare *w) EV_THROW	4987	ev_prepare_stop (EV_P_ ev_prepare *w) EV_NOEXCEPT
4399	{	4988	{
4400	clear_pending (EV_A_ (W)w);	4989	clear_pending (EV_A_ (W)w);
4401	if (expect_false (!ev_is_active (w)))	4990	if (ecb_expect_false (!ev_is_active (w)))
4402	return;	4991	return;
4403		4992
4404	EV_FREQUENT_CHECK;	4993	EV_FREQUENT_CHECK;
4405		4994
4406	{	4995	{
…		…
4416	}	5005	}
4417	#endif	5006	#endif
4418		5007
4419	#if EV_CHECK_ENABLE	5008	#if EV_CHECK_ENABLE
4420	void	5009	void
4421	ev_check_start (EV_P_ ev_check *w) EV_THROW	5010	ev_check_start (EV_P_ ev_check *w) EV_NOEXCEPT
4422	{	5011	{
4423	if (expect_false (ev_is_active (w)))	5012	if (ecb_expect_false (ev_is_active (w)))
4424	return;	5013	return;
4425		5014
4426	EV_FREQUENT_CHECK;	5015	EV_FREQUENT_CHECK;
4427		5016
4428	ev_start (EV_A_ (W)w, ++checkcnt);	5017	ev_start (EV_A_ (W)w, ++checkcnt);
4429	array_needsize (ev_check *, checks, checkmax, checkcnt, EMPTY2);	5018	array_needsize (ev_check *, checks, checkmax, checkcnt, array_needsize_noinit);
4430	checks [checkcnt - 1] = w;	5019	checks [checkcnt - 1] = w;
4431		5020
4432	EV_FREQUENT_CHECK;	5021	EV_FREQUENT_CHECK;
4433	}	5022	}
4434		5023
4435	void	5024	void
4436	ev_check_stop (EV_P_ ev_check *w) EV_THROW	5025	ev_check_stop (EV_P_ ev_check *w) EV_NOEXCEPT
4437	{	5026	{
4438	clear_pending (EV_A_ (W)w);	5027	clear_pending (EV_A_ (W)w);
4439	if (expect_false (!ev_is_active (w)))	5028	if (ecb_expect_false (!ev_is_active (w)))
4440	return;	5029	return;
4441		5030
4442	EV_FREQUENT_CHECK;	5031	EV_FREQUENT_CHECK;
4443		5032
4444	{	5033	{
…		…
4453	EV_FREQUENT_CHECK;	5042	EV_FREQUENT_CHECK;
4454	}	5043	}
4455	#endif	5044	#endif
4456		5045
4457	#if EV_EMBED_ENABLE	5046	#if EV_EMBED_ENABLE
4458	void noinline	5047	ecb_noinline
		5048	void
4459	ev_embed_sweep (EV_P_ ev_embed *w) EV_THROW	5049	ev_embed_sweep (EV_P_ ev_embed *w) EV_NOEXCEPT
4460	{	5050	{
4461	ev_run (w->other, EVRUN_NOWAIT);	5051	ev_run (w->other, EVRUN_NOWAIT);
4462	}	5052	}
4463		5053
4464	static void	5054	static void
…		…
4512	ev_idle_stop (EV_A_ idle);	5102	ev_idle_stop (EV_A_ idle);
4513	}	5103	}
4514	#endif	5104	#endif
4515		5105
4516	void	5106	void
4517	ev_embed_start (EV_P_ ev_embed *w) EV_THROW	5107	ev_embed_start (EV_P_ ev_embed *w) EV_NOEXCEPT
4518	{	5108	{
4519	if (expect_false (ev_is_active (w)))	5109	if (ecb_expect_false (ev_is_active (w)))
4520	return;	5110	return;
4521		5111
4522	{	5112	{
4523	EV_P = w->other;	5113	EV_P = w->other;
4524	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));	5114	assert (("libev: loop to be embedded is not embeddable", backend & ev_embeddable_backends ()));
…		…
4543		5133
4544	EV_FREQUENT_CHECK;	5134	EV_FREQUENT_CHECK;
4545	}	5135	}
4546		5136
4547	void	5137	void
4548	ev_embed_stop (EV_P_ ev_embed *w) EV_THROW	5138	ev_embed_stop (EV_P_ ev_embed *w) EV_NOEXCEPT
4549	{	5139	{
4550	clear_pending (EV_A_ (W)w);	5140	clear_pending (EV_A_ (W)w);
4551	if (expect_false (!ev_is_active (w)))	5141	if (ecb_expect_false (!ev_is_active (w)))
4552	return;	5142	return;
4553		5143
4554	EV_FREQUENT_CHECK;	5144	EV_FREQUENT_CHECK;
4555		5145
4556	ev_io_stop (EV_A_ &w->io);	5146	ev_io_stop (EV_A_ &w->io);
…		…
4563	}	5153	}
4564	#endif	5154	#endif
4565		5155
4566	#if EV_FORK_ENABLE	5156	#if EV_FORK_ENABLE
4567	void	5157	void
4568	ev_fork_start (EV_P_ ev_fork *w) EV_THROW	5158	ev_fork_start (EV_P_ ev_fork *w) EV_NOEXCEPT
4569	{	5159	{
4570	if (expect_false (ev_is_active (w)))	5160	if (ecb_expect_false (ev_is_active (w)))
4571	return;	5161	return;
4572		5162
4573	EV_FREQUENT_CHECK;	5163	EV_FREQUENT_CHECK;
4574		5164
4575	ev_start (EV_A_ (W)w, ++forkcnt);	5165	ev_start (EV_A_ (W)w, ++forkcnt);
4576	array_needsize (ev_fork *, forks, forkmax, forkcnt, EMPTY2);	5166	array_needsize (ev_fork *, forks, forkmax, forkcnt, array_needsize_noinit);
4577	forks [forkcnt - 1] = w;	5167	forks [forkcnt - 1] = w;
4578		5168
4579	EV_FREQUENT_CHECK;	5169	EV_FREQUENT_CHECK;
4580	}	5170	}
4581		5171
4582	void	5172	void
4583	ev_fork_stop (EV_P_ ev_fork *w) EV_THROW	5173	ev_fork_stop (EV_P_ ev_fork *w) EV_NOEXCEPT
4584	{	5174	{
4585	clear_pending (EV_A_ (W)w);	5175	clear_pending (EV_A_ (W)w);
4586	if (expect_false (!ev_is_active (w)))	5176	if (ecb_expect_false (!ev_is_active (w)))
4587	return;	5177	return;
4588		5178
4589	EV_FREQUENT_CHECK;	5179	EV_FREQUENT_CHECK;
4590		5180
4591	{	5181	{
…		…
4601	}	5191	}
4602	#endif	5192	#endif
4603		5193
4604	#if EV_CLEANUP_ENABLE	5194	#if EV_CLEANUP_ENABLE
4605	void	5195	void
4606	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_THROW	5196	ev_cleanup_start (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4607	{	5197	{
4608	if (expect_false (ev_is_active (w)))	5198	if (ecb_expect_false (ev_is_active (w)))
4609	return;	5199	return;
4610		5200
4611	EV_FREQUENT_CHECK;	5201	EV_FREQUENT_CHECK;
4612		5202
4613	ev_start (EV_A_ (W)w, ++cleanupcnt);	5203	ev_start (EV_A_ (W)w, ++cleanupcnt);
4614	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, EMPTY2);	5204	array_needsize (ev_cleanup *, cleanups, cleanupmax, cleanupcnt, array_needsize_noinit);
4615	cleanups [cleanupcnt - 1] = w;	5205	cleanups [cleanupcnt - 1] = w;
4616		5206
4617	/* cleanup watchers should never keep a refcount on the loop */	5207	/* cleanup watchers should never keep a refcount on the loop */
4618	ev_unref (EV_A);	5208	ev_unref (EV_A);
4619	EV_FREQUENT_CHECK;	5209	EV_FREQUENT_CHECK;
4620	}	5210	}
4621		5211
4622	void	5212	void
4623	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_THROW	5213	ev_cleanup_stop (EV_P_ ev_cleanup *w) EV_NOEXCEPT
4624	{	5214	{
4625	clear_pending (EV_A_ (W)w);	5215	clear_pending (EV_A_ (W)w);
4626	if (expect_false (!ev_is_active (w)))	5216	if (ecb_expect_false (!ev_is_active (w)))
4627	return;	5217	return;
4628		5218
4629	EV_FREQUENT_CHECK;	5219	EV_FREQUENT_CHECK;
4630	ev_ref (EV_A);	5220	ev_ref (EV_A);
4631		5221
…		…
4642	}	5232	}
4643	#endif	5233	#endif
4644		5234
4645	#if EV_ASYNC_ENABLE	5235	#if EV_ASYNC_ENABLE
4646	void	5236	void
4647	ev_async_start (EV_P_ ev_async *w) EV_THROW	5237	ev_async_start (EV_P_ ev_async *w) EV_NOEXCEPT
4648	{	5238	{
4649	if (expect_false (ev_is_active (w)))	5239	if (ecb_expect_false (ev_is_active (w)))
4650	return;	5240	return;
4651		5241
4652	w->sent = 0;	5242	w->sent = 0;
4653		5243
4654	evpipe_init (EV_A);	5244	evpipe_init (EV_A);
4655		5245
4656	EV_FREQUENT_CHECK;	5246	EV_FREQUENT_CHECK;
4657		5247
4658	ev_start (EV_A_ (W)w, ++asynccnt);	5248	ev_start (EV_A_ (W)w, ++asynccnt);
4659	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, EMPTY2);	5249	array_needsize (ev_async *, asyncs, asyncmax, asynccnt, array_needsize_noinit);
4660	asyncs [asynccnt - 1] = w;	5250	asyncs [asynccnt - 1] = w;
4661		5251
4662	EV_FREQUENT_CHECK;	5252	EV_FREQUENT_CHECK;
4663	}	5253	}
4664		5254
4665	void	5255	void
4666	ev_async_stop (EV_P_ ev_async *w) EV_THROW	5256	ev_async_stop (EV_P_ ev_async *w) EV_NOEXCEPT
4667	{	5257	{
4668	clear_pending (EV_A_ (W)w);	5258	clear_pending (EV_A_ (W)w);
4669	if (expect_false (!ev_is_active (w)))	5259	if (ecb_expect_false (!ev_is_active (w)))
4670	return;	5260	return;
4671		5261
4672	EV_FREQUENT_CHECK;	5262	EV_FREQUENT_CHECK;
4673		5263
4674	{	5264	{
…		…
4682		5272
4683	EV_FREQUENT_CHECK;	5273	EV_FREQUENT_CHECK;
4684	}	5274	}
4685		5275
4686	void	5276	void
4687	ev_async_send (EV_P_ ev_async *w) EV_THROW	5277	ev_async_send (EV_P_ ev_async *w) EV_NOEXCEPT
4688	{	5278	{
4689	w->sent = 1;	5279	w->sent = 1;
4690	evpipe_write (EV_A_ &async_pending);	5280	evpipe_write (EV_A_ &async_pending);
4691	}	5281	}
4692	#endif	5282	#endif
…		…
4729		5319
4730	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));	5320	once_cb (EV_A_ once, revents | ev_clear_pending (EV_A_ &once->io));
4731	}	5321	}
4732		5322
4733	void	5323	void
4734	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_THROW	5324	ev_once (EV_P_ int fd, int events, ev_tstamp timeout, void (*cb)(int revents, void *arg), void *arg) EV_NOEXCEPT
4735	{	5325	{
4736	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));	5326	struct ev_once *once = (struct ev_once *)ev_malloc (sizeof (struct ev_once));
4737
4738	if (expect_false (!once))
4739	{
4740	cb (EV_ERROR | EV_READ | EV_WRITE | EV_TIMER, arg);
4741	return;
4742	}
4743		5327
4744	once->cb = cb;	5328	once->cb = cb;
4745	once->arg = arg;	5329	once->arg = arg;
4746		5330
4747	ev_init (&once->io, once_cb_io);	5331	ev_init (&once->io, once_cb_io);
…		…
4760	}	5344	}
4761		5345
4762	/*****************************************************************************/	5346	/*****************************************************************************/
4763		5347
4764	#if EV_WALK_ENABLE	5348	#if EV_WALK_ENABLE
4765	void ecb_cold	5349	ecb_cold
		5350	void
4766	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_THROW	5351	ev_walk (EV_P_ int types, void (*cb)(EV_P_ int type, void *w)) EV_NOEXCEPT
4767	{	5352	{
4768	int i, j;	5353	int i, j;
4769	ev_watcher_list *wl, *wn;	5354	ev_watcher_list *wl, *wn;
4770		5355
4771	if (types & (EV_IO | EV_EMBED))	5356	if (types & (EV_IO | EV_EMBED))

Diff Legend

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