| /f-stack/freebsd/contrib/openzfs/lib/libspl/include/os/linux/sys/ |
| H A D | sysmacros.h | 34 #define MIN(a, b) ((a) < (b) ? (a) : (b)) argument 37 #define MAX(a, b) ((a) < (b) ? (b) : (a)) argument 40 #define ABS(a) ((a) < 0 ? -(a) : (a)) argument 43 #define ARRAY_SIZE(a) (sizeof (a) / sizeof (a[0])) argument 50 #define _sysconf(a) sysconf(a) argument 62 #define P2NPHASE_TYPED(x, align, type) \ argument 65 #define IS_P2ALIGNED(v, a) ((((uintptr_t)(v)) & ((uintptr_t)(a) - 1)) == 0) argument 78 #define P2ALIGN_TYPED(x, align, type) \ argument 80 #define P2PHASE_TYPED(x, align, type) \ argument 86 #define P2END_TYPED(x, align, type) \ argument [all …]
|
| /f-stack/freebsd/sys/ |
| H A D | libkern.h | 91 static __inline int imax(int a, int b) { return (a > b ? a : b); } in imax() 92 static __inline int imin(int a, int b) { return (a < b ? a : b); } in imin() 103 static __inline __uintmax_t ummax(__uintmax_t a, __uintmax_t b) in ummax() 108 static __inline __uintmax_t ummin(__uintmax_t a, __uintmax_t b) in ummin() 115 static __inline int abs(int a) { return (a < 0 ? -a : a); } in abs() 116 static __inline long labs(long a) { return (a < 0 ? -a : a); } in labs() 153 #define bitcount64(x) __bitcount64((uint64_t)(x)) argument 154 #define bitcount32(x) __bitcount32((uint32_t)(x)) argument 155 #define bitcount16(x) __bitcount16((uint16_t)(x)) argument 156 #define bitcountl(x) __bitcountl((u_long)(x)) argument [all …]
|
| H A D | param.h | 204 #define ctob(x) ((x)<<PAGE_SHIFT) argument 295 #define setbit(a,i) (((unsigned char *)(a))[(i)/NBBY] |= 1<<((i)%NBBY)) argument 296 #define clrbit(a,i) (((unsigned char *)(a))[(i)/NBBY] &= ~(1<<((i)%NBBY))) argument 297 #define isset(a,i) \ argument 299 #define isclr(a,i) \ argument 314 #define MIN(a,b) (((a)<(b))?(a):(b)) argument 315 #define MAX(a,b) (((a)>(b))?(a):(b)) argument 335 #define htonl(x) __htonl(x) argument 336 #define htons(x) __htons(x) argument 337 #define ntohl(x) __ntohl(x) argument [all …]
|
| H A D | tslog.h | 43 #define TSENTER2(x) TSRAW(curthread, TS_ENTER, __func__, x) argument 45 #define TSEXIT2(x) TSRAW(curthread, TS_EXIT, __func__, x) argument 46 #define TSTHREAD(td, x) TSRAW(td, TS_THREAD, x, NULL) argument 47 #define TSEVENT(x) TSRAW(curthread, TS_EVENT, x, NULL) argument 48 #define TSEVENT2(x, y) TSRAW(curthread, TS_EVENT, x, y) argument 50 #define TSWAIT(x) TSEVENT2("WAIT", x); argument 51 #define TSUNWAIT(x) TSEVENT2("UNWAIT", x); argument 52 #define TSHOLD(x) TSEVENT2("HOLD", x); argument 53 #define TSRELEASE(x) TSEVENT2("RELEASE", x); argument 56 #define TSRAW(a, b, c, d) tslog(a, b, c, d) argument [all …]
|
| /f-stack/dpdk/drivers/raw/ifpga/base/ |
| H A D | opae_osdep.h | 39 #define BIT(a) (1UL << (a)) argument 42 #define BIT_ULL(a) (1ULL << (a)) argument 56 #define dev_err(x, args...) dev_printf(ERR, args) argument 57 #define dev_info(x, args...) dev_printf(INFO, args) argument 59 #define dev_debug(x, args...) dev_printf(DEBUG, args) argument 66 #define WARN_ON(x) do { \ argument 74 #define udelay(x) opae_udelay(x) argument 75 #define msleep(x) opae_udelay(1000 * (x)) argument 78 #define time_after(a, b) ((long)((b) - (a)) < 0) argument 79 #define time_before(a, b) time_after(b, a) argument [all …]
|
| H A D | ifpga_compat.h | 20 #define IFPGA_ALIGN(x, a) (((x) + (a) - 1) & ~((a) - 1)) argument 22 #define IS_ALIGNED(x, a) (((x) & ((typeof(x))(a) - 1)) == 0) argument 56 #define UNUSED(x) (void)(x) argument
|
| /f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/ |
| H A D | blake2b-compress-avx2.h | 30 #define ADD(a, b) _mm256_add_epi64(a, b) argument 31 #define SUB(a, b) _mm256_sub_epi64(a, b) argument 33 #define XOR(a, b) _mm256_xor_si256(a, b) argument 34 #define AND(a, b) _mm256_and_si256(a, b) argument 35 #define OR(a, b) _mm256_or_si256(a, b) argument 37 #define ROT32(x) _mm256_shuffle_epi32((x), _MM_SHUFFLE(2, 3, 0, 1)) argument 38 #define ROT24(x) _mm256_shuffle_epi8((x), ROTATE24) argument 39 #define ROT16(x) _mm256_shuffle_epi8((x), ROTATE16) argument 40 #define ROT63(x) _mm256_or_si256(_mm256_srli_epi64((x), 63), ADD((x), (x))) argument 42 #define BLAKE2B_G1_V1(a, b, c, d, m) \ argument [all …]
|
| /f-stack/freebsd/contrib/openzfs/include/os/freebsd/spl/sys/ |
| H A D | ccompile.h | 135 #define EXPORT_SYMBOL(x) argument 139 #define module_param(a, b, c) argument 140 #define module_param_call(a, b, c, d, e) argument 141 #define module_param_named(a, b, c, d) argument 142 #define MODULE_PARM_DESC(a, b) argument 185 #define param_set_charp(a, b) (0) argument 221 #define ARRAY_SIZE(a) (sizeof (a) / sizeof (a[0])) argument 242 #define IS_P2ALIGNED(v, a) ((((uintptr_t)(v)) & ((uintptr_t)(a) - 1)) == 0) argument 258 #define P2ALIGN_TYPED(x, align, type) \ argument 260 #define P2PHASE_TYPED(x, align, type) \ argument [all …]
|
| H A D | sysmacros.h | 57 #define MIN(a, b) ((a) < (b) ? (a) : (b)) argument 60 #define MAX(a, b) ((a) < (b) ? (b) : (a)) argument 63 #define ABS(a) ((a) < 0 ? -(a) : (a)) argument 66 #define SIGNOF(a) ((a) < 0 ? -1 : (a) > 0) argument 69 #define ARRAY_SIZE(a) (sizeof (a) / sizeof (a[0])) argument 137 #define DEVCMPL(x) (x) argument 142 #define DEVCMPL(x) \ argument 147 #define DEVEXPL(x) \ argument 155 #define cmpdev(x) \ argument 162 #define expdev(x) \ argument [all …]
|
| /f-stack/freebsd/kern/ |
| H A D | md5c.c | 98 #define F(x, y, z) (((x) & (y)) | ((~x) & (z))) argument 99 #define G(x, y, z) (((x) & (z)) | ((y) & (~z))) argument 100 #define H(x, y, z) ((x) ^ (y) ^ (z)) argument 101 #define I(x, y, z) ((y) ^ ((x) | (~z))) argument 104 #define ROTATE_LEFT(x, n) (((x) << (n)) | ((x) >> (32-(n)))) argument 110 #define FF(a, b, c, d, x, s, ac) { \ argument 115 #define GG(a, b, c, d, x, s, ac) { \ argument 120 #define HH(a, b, c, d, x, s, ac) { \ argument 125 #define II(a, b, c, d, x, s, ac) { \ argument 239 u_int32_t a = state[0], b = state[1], c = state[2], d = state[3], x[16]; local
|
| H A D | md4c.c | 70 #define F(x, y, z) (((x) & (y)) | ((~x) & (z))) argument 71 #define G(x, y, z) (((x) & (y)) | ((x) & (z)) | ((y) & (z))) argument 72 #define H(x, y, z) ((x) ^ (y) ^ (z)) argument 76 #define ROTATE_LEFT(x, n) (((x) << (n)) | ((x) >> (32-(n)))) argument 80 #define FF(a, b, c, d, x, s) { \ argument 84 #define GG(a, b, c, d, x, s) { \ argument 88 #define HH(a, b, c, d, x, s) { \ argument 187 UINT4 a = state[0], b = state[1], c = state[2], d = state[3], x[16]; in MD4Transform() local
|
| /f-stack/freebsd/contrib/openzfs/include/os/freebsd/linux/ |
| H A D | compiler.h | 43 #define __chk_user_ptr(x) ((void)0) argument 44 #define __chk_io_ptr(x) ((void)0) argument 46 #define __acquires(x) argument 47 #define __releases(x) argument 50 #define __cond_lock(x, c) (c) argument 75 #define typeof(x) __typeof(x) argument 77 #define uninitialized_var(x) x = x argument 82 #define __printf(a, b) __printflike(a, b) argument 86 #define ___PASTE(a, b) a##b argument 87 #define __PASTE(a, b) ___PASTE(a, b) argument [all …]
|
| /f-stack/dpdk/lib/librte_eal/arm/include/ |
| H A D | rte_vect.h | 25 xmm_t x; member 36 vqtbl1q_u8(uint8x16_t a, uint8x16_t b) in vqtbl1q_u8() 56 vaddvq_u16(uint16x8_t a) in vaddvq_u16() 73 vcopyq_laneq_u32(uint32x4_t a, const int lane_a, in vcopyq_laneq_u32() 89 vceqzq_u32(uint32x4_t a) in vceqzq_u32() 97 vreinterpretq_u64_p128(poly128_t x) in vreinterpretq_u64_p128() 104 vreinterpretq_p64_u64(uint64x2_t x) in vreinterpretq_p64_u64() 111 vgetq_lane_p64(poly64x2_t x, const int lane) in vgetq_lane_p64()
|
| /f-stack/dpdk/drivers/net/i40e/base/ |
| H A D | i40e_osdep.h | 39 #define low_16_bits(x) ((x) & 0xFFFF) argument 40 #define high_16_bits(x) (((x) & 0xFFFF0000) >> 16) argument 70 #define min(a,b) RTE_MIN(a,b) argument 71 #define max(a,b) RTE_MAX(a,b) argument 129 #define I40E_PCI_REG_ADDR(a, reg) \ argument 154 #define wr32(a, reg, value) \ argument 213 #define DELAY(x) rte_delay_us_sleep(x) argument 214 #define i40e_usec_delay(x) DELAY(x) argument 215 #define i40e_msec_delay(x) DELAY(1000 * (x)) argument 216 #define udelay(x) DELAY(x) argument [all …]
|
| /f-stack/freebsd/contrib/ipfilter/netinet/ |
| H A D | ip_compat.h | 39 # define bzero(a,b) memset(a,0,b) argument 41 # define bcopy(a,b,c) memmove(b,a,c) argument 111 # define COPYIN(a,b,c) copyin((caddr_t)(a), (caddr_t)(b), (c)) argument 354 # define KMALLOC(a,b) (a) = (b)malloc(sizeof(*a)) argument 355 # define KMALLOCS(a,b,c) (a) = (b)malloc(c) argument 361 # define COPYIN(a,b,c) bcopywrap((a), (b), (c)) argument 362 # define COPYOUT(a,b,c) bcopywrap((a), (b), (c)) argument 368 # define UIOMOVE(a,b,c,d) ipfuiomove((caddr_t)a,b,c,d) argument 451 # define MAX(a,b) (((a) > (b)) ? (a) : (b)) argument 501 # define UIOMOVE(a,b,c,d) uiomove((caddr_t)a,b,d) argument [all …]
|
| /f-stack/freebsd/contrib/openzfs/include/os/linux/spl/sys/ |
| H A D | sysmacros.h | 124 #define highbit(x) __fls(x) argument 125 #define lowbit(x) __ffs(x) argument 127 #define highbit64(x) fls64(x) argument 132 #define MIN(a, b) ((a) < (b) ? (a) : (b)) argument 135 #define MAX(a, b) ((a) < (b) ? (b) : (a)) argument 138 #define ABS(a) ((a) < 0 ? -(a) : (a)) argument 159 #define IS_P2ALIGNED(v, a) ((((uintptr_t)(v)) & ((uintptr_t)(a) - 1)) == 0) argument 175 #define P2ALIGN_TYPED(x, align, type) \ argument 177 #define P2PHASE_TYPED(x, align, type) \ argument 179 #define P2NPHASE_TYPED(x, align, type) \ argument [all …]
|
| H A D | debug.h | 51 #define __printflike(a, b) __printf(a, b) argument 62 #define PANIC(fmt, a...) \ argument 125 #define CTASSERT(x) { _CTASSERT(x, __LINE__); } argument 126 #define _CTASSERT(x, y) __CTASSERT(x, y) argument 127 #define __CTASSERT(x, y) \ argument 136 #define ASSERT(x) ((void)0) argument 137 #define ASSERT3B(x,y,z) ((void)0) argument 138 #define ASSERT3S(x,y,z) ((void)0) argument 139 #define ASSERT3U(x,y,z) ((void)0) argument 140 #define ASSERT3P(x,y,z) ((void)0) argument [all …]
|
| /f-stack/freebsd/opencrypto/ |
| H A D | gfmult.h | 37 #define __aligned(x) __attribute__((__aligned__(x))) argument 39 #define be64enc(buf, x) (*(uint64_t *)buf = __builtin_bswap64(x)) argument 83 #define MAKE_GF128(a, b) ((struct gf128){.v = { (a), (b) } }) argument 84 #define GF128_EQ(a, b) ((((a).v[0] ^ (b).v[0]) | \ argument 112 gf128_add(struct gf128 a, struct gf128 b) in gf128_add()
|
| /f-stack/freebsd/libkern/ |
| H A D | qsort.c | 60 #define SWAPINIT(TYPE, a, es) swaptype_ ## TYPE = \ argument 65 swapfunc(char *a, char *b, size_t n, int swaptype_long, int swaptype_int) in swapfunc() 75 #define swap(a, b) \ argument 87 #define vecswap(a, b, n) \ argument 91 #define CMP(t, x, y) (cmp((t), (x), (y))) argument 93 #define CMP(t, x, y) (cmp((x), (y))) argument 97 med3(char *a, char *b, char *c, cmp_t *cmp, void *thunk in med3() 110 qsort_r(void *a, size_t n, size_t es, void *thunk, cmp_t *cmp) in qsort_r()
|
| /f-stack/dpdk/drivers/net/cxgbe/ |
| H A D | cxgbe_compat.h | 31 #define dev_err(x, fmt, ...) \ argument 33 #define dev_info(x, fmt, ...) \ argument 35 #define dev_warn(x, fmt, ...) \ argument 51 #define ASSERT(x) do {\ argument 55 #define BUG_ON(x) ASSERT(!(x)) argument 58 #define WARN_ON(x) do { \ argument 75 #define CXGBE_ALIGN(x, a) (((x) + (a) - 1) & ~((a) - 1)) argument 76 #define PTR_ALIGN(p, a) ((typeof(p))CXGBE_ALIGN((unsigned long)(p), (a))) argument 127 #define min(a, b) RTE_MIN(a, b) argument 131 #define max(a, b) RTE_MAX(a, b) argument [all …]
|
| /f-stack/freebsd/contrib/dpdk_rte_lpm/ |
| H A D | rte_jhash.h | 39 #define rot(x, k) (((x) << (k)) | ((x) >> (32-(k)))) argument 42 #define __rte_jhash_mix(a, b, c) do { \ argument 51 #define __rte_jhash_final(a, b, c) do { \ argument 65 #define BIT_SHIFT(x, y, k) (((x) >> (k)) | ((uint64_t)(y) << (32-(k)))) argument 78 uint32_t a, b, c; in __rte_jhash_2hashes() local 307 __rte_jhash_3words(uint32_t a, uint32_t b, uint32_t c, uint32_t initval) in __rte_jhash_3words() 334 rte_jhash_3words(uint32_t a, uint32_t b, uint32_t c, uint32_t initval) in rte_jhash_3words() 353 rte_jhash_2words(uint32_t a, uint32_t b, uint32_t initval) in rte_jhash_2words() 370 rte_jhash_1word(uint32_t a, uint32_t initval) in rte_jhash_1word()
|
| /f-stack/dpdk/lib/librte_hash/ |
| H A D | rte_jhash.h | 45 #define rot(x, k) (((x) << (k)) | ((x) >> (32-(k)))) argument 48 #define __rte_jhash_mix(a, b, c) do { \ argument 57 #define __rte_jhash_final(a, b, c) do { \ argument 71 #define BIT_SHIFT(x, y, k) (((x) >> (k)) | ((uint64_t)(y) << (32-(k)))) argument 84 uint32_t a, b, c; in __rte_jhash_2hashes() local 313 __rte_jhash_3words(uint32_t a, uint32_t b, uint32_t c, uint32_t initval) in __rte_jhash_3words() 340 rte_jhash_3words(uint32_t a, uint32_t b, uint32_t c, uint32_t initval) in rte_jhash_3words() 359 rte_jhash_2words(uint32_t a, uint32_t b, uint32_t initval) in rte_jhash_2words() 376 rte_jhash_1word(uint32_t a, uint32_t initval) in rte_jhash_1word()
|
| /f-stack/dpdk/drivers/raw/ifpga/base/osdep_rte/ |
| H A D | osdep_generic.h | 22 #define opae_udelay(x) rte_delay_us(x) argument 39 #define min(a, b) RTE_MIN(a, b) argument 40 #define max(a, b) RTE_MAX(a, b) argument 43 #define spinlock_init(x) rte_spinlock_init(x) argument 44 #define spinlock_lock(x) rte_spinlock_lock(x) argument 45 #define spinlock_unlock(x) rte_spinlock_unlock(x) argument 54 #define opae_memcpy(a, b, c) rte_memcpy((a), (b), (c)) argument
|
| /f-stack/freebsd/contrib/zstd/lib/freebsd/ |
| H A D | stdlib.h | 39 #define malloc(x) (malloc)((x), M_ZSTD, M_WAITOK) argument 40 #define free(x) (free)((x), M_ZSTD) argument 41 #define calloc(a, b) (mallocarray)((a), (b), M_ZSTD, M_WAITOK | M_ZERO) argument
|
| /f-stack/freebsd/mips/include/ |
| H A D | asm.h | 103 #define AENT(x) \ argument 106 #define AENT(x) argument 212 #define END(x) \ argument 545 #define SETUP_GP64(a,b) /* n32/n64 specific */ argument 546 #define SETUP_GP64_R(a,b) /* n32/n64 specific */ argument 547 #define SETUP_GPX64(a,b) /* n32/n64 specific */ argument 550 #define USE_ALT_CP(a) /* n32/n64 specific */ argument 567 #define SETUP_GP64(a,b) .cpsetup $25, a, b argument 568 #define SETUP_GPX64(a,b) \ argument 577 #define SETUP_GPX64_L(a,b,c) \ argument [all …]
|