/dpdk/lib/eal/ppc/include/ |
H A D | rte_byteorder.h | 54 #define rte_bswap16(x) ((uint16_t)(__builtin_constant_p(x) ? \ argument 58 #define rte_bswap32(x) ((uint32_t)(__builtin_constant_p(x) ? \ argument 62 #define rte_bswap64(x) ((uint64_t)(__builtin_constant_p(x) argument 72 rte_cpu_to_le_16(x) global() argument 73 rte_cpu_to_le_32(x) global() argument 74 rte_cpu_to_le_64(x) global() argument 76 rte_cpu_to_be_16(x) global() argument 77 rte_cpu_to_be_32(x) global() argument 78 rte_cpu_to_be_64(x) global() argument 80 rte_le_to_cpu_16(x) global() argument 81 rte_le_to_cpu_32(x) global() argument 82 rte_le_to_cpu_64(x) global() argument 84 rte_be_to_cpu_16(x) global() argument 85 rte_be_to_cpu_32(x) global() argument 86 rte_be_to_cpu_64(x) global() argument 90 rte_cpu_to_le_16(x) global() argument 91 rte_cpu_to_le_32(x) global() argument 92 rte_cpu_to_le_64(x) global() argument 94 rte_cpu_to_be_16(x) global() argument 95 rte_cpu_to_be_32(x) global() argument 96 rte_cpu_to_be_64(x) global() argument 98 rte_le_to_cpu_16(x) global() argument 99 rte_le_to_cpu_32(x) global() argument 100 rte_le_to_cpu_64(x) global() argument 102 rte_be_to_cpu_16(x) global() argument 103 rte_be_to_cpu_32(x) global() argument 104 rte_be_to_cpu_64(x) global() argument [all...] |
/dpdk/lib/eal/x86/include/ |
H A D | rte_byteorder.h | 29 uint16_t x = _x; in rte_arch_bswap16() local 44 uint32_t x = _x; in rte_arch_bswap32() local 55 #define rte_bswap16(x) ((uint16_ argument 51 rte_bswap16(x) global() argument 59 rte_bswap64(x) global() argument 70 rte_cpu_to_le_16(x) global() argument 71 rte_cpu_to_le_32(x) global() argument 72 rte_cpu_to_le_64(x) global() argument 74 rte_cpu_to_be_16(x) global() argument 75 rte_cpu_to_be_32(x) global() argument 76 rte_cpu_to_be_64(x) global() argument 78 rte_le_to_cpu_16(x) global() argument 79 rte_le_to_cpu_32(x) global() argument 80 rte_le_to_cpu_64(x) global() argument 82 rte_be_to_cpu_16(x) global() argument 83 rte_be_to_cpu_32(x) global() argument 84 rte_be_to_cpu_64(x) global() argument [all...] |
/dpdk/lib/eal/loongarch/include/ |
H A D | rte_byteorder.h | 16 #define rte_cpu_to_le_16(x) (x) argument 17 #define rte_cpu_to_le_32(x) (x) argument 18 #define rte_cpu_to_le_64(x) (x) argument 20 #define rte_cpu_to_be_16(x) rte_bswap16(x) argument 21 #define rte_cpu_to_be_32(x) rte_bswap32(x) argument 22 rte_cpu_to_be_64(x) global() argument 24 rte_le_to_cpu_16(x) global() argument 25 rte_le_to_cpu_32(x) global() argument 26 rte_le_to_cpu_64(x) global() argument 28 rte_be_to_cpu_16(x) global() argument 29 rte_be_to_cpu_32(x) global() argument 30 rte_be_to_cpu_64(x) global() argument [all...] |
/dpdk/lib/eal/arm/include/ |
H A D | rte_byteorder.h | 23 #define rte_cpu_to_le_16(x) (x) argument 24 #define rte_cpu_to_le_32(x) (x) argument 25 #define rte_cpu_to_le_64(x) (x) argument 27 #define rte_cpu_to_be_16(x) rte_bswap16(x) argument 28 #define rte_cpu_to_be_32(x) rte_bswap32(x) argument 29 rte_cpu_to_be_64(x) global() argument 31 rte_le_to_cpu_16(x) global() argument 32 rte_le_to_cpu_32(x) global() argument 33 rte_le_to_cpu_64(x) global() argument 35 rte_be_to_cpu_16(x) global() argument 36 rte_be_to_cpu_32(x) global() argument 37 rte_be_to_cpu_64(x) global() argument [all...] |
/dpdk/lib/eal/riscv/include/ |
H A D | rte_byteorder.h | 23 #define rte_cpu_to_le_16(x) (x) argument 24 #define rte_cpu_to_le_32(x) (x) argument 25 #define rte_cpu_to_le_64(x) (x) argument 27 #define rte_cpu_to_be_16(x) rte_bswap16(x) argument 28 #define rte_cpu_to_be_32(x) rte_bswap32(x) argument 29 rte_cpu_to_be_64(x) global() argument 31 rte_le_to_cpu_16(x) global() argument 32 rte_le_to_cpu_32(x) global() argument 33 rte_le_to_cpu_64(x) global() argument 35 rte_be_to_cpu_16(x) global() argument 36 rte_be_to_cpu_32(x) global() argument 37 rte_be_to_cpu_64(x) global() argument [all...] |
/dpdk/drivers/net/cxgbe/base/ |
H A D | t4_regs.h | 50 #define V_DATAPORTNUM(x) ((x) << S_DATAPORTNUM) argument 54 #define V_DATALKPTYPE(x) ((x) << S_DATALKPTYPE) argument 64 #define V_QID(x) ((x) << S_QID) argument 65 #define G_QID(x) (((x) >> S_QID) & M_QID) argument 68 #define V_DBPRIO(x) ((x) << S_DBPRIO) argument 73 #define V_PIDX(x) ((x) << S_PIDX) argument 74 #define G_PIDX(x) (((x) >> S_PIDX) & M_PIDX) argument 77 #define V_DBTYPE(x) ((x) << S_DBTYPE) argument 82 #define V_PIDX_T5(x) ((x) << S_PIDX_T5) argument 83 #define G_PIDX_T5(x) (((x) >> S_PIDX_T5) & M_PIDX_T5) argument [all …]
|
H A D | t4fw_interface.h | 80 #define V_FW_WR_OP(x) ((x) << S_FW_WR_OP) argument 81 #define G_FW_WR_OP(x) (((x) >> S_FW_WR_OP) & M_FW_WR_OP) argument 86 #define V_FW_WR_ATOMIC(x) ((x) << S_FW_WR_ATOMIC) argument 92 #define V_FW_WR_IMMDLEN(x) ((x) << S_FW_WR_IMMDLEN) argument 93 #define G_FW_WR_IMMDLEN(x) \ argument 100 #define V_FW_WR_EQUEQ(x) ((x) << S_FW_WR_EQUEQ) argument 101 #define G_FW_WR_EQUEQ(x) (((x) >> S_FW_WR_EQUEQ) & M_FW_WR_EQUEQ) argument 107 #define V_FW_WR_FLOWID(x) ((x) << S_FW_WR_FLOWID) argument 113 #define V_FW_WR_LEN16(x) ((x) << S_FW_WR_LEN16) argument 114 #define G_FW_WR_LEN16(x) (((x) >> S_FW_WR_LEN16) & M_FW_WR_LEN16) argument [all …]
|
H A D | t4_msg.h | 57 #define V_CPL_OPCODE(x) ((x) << S_CPL_OPCODE) argument 59 #define G_TID(x) ((x) & 0xFFFFFF) argument 72 #define G_TID_TID(x) (((x) >> S_TID_TID) & M_TID_TID) argument 75 #define V_TID_QID(x) ((x) << S_TID_QID) argument 120 #define V_COOKIE(x) ((x) << S_COOKIE) argument 121 #define G_COOKIE(x) (((x) >> S_COOKIE) & M_COOKIE) argument 125 #define V_TX_CHAN(x) ((x) << S_TX_CHAN) argument 128 #define V_DELACK(x) ((x) << S_DELACK) argument 131 #define V_NON_OFFLOAD(x) ((x) << S_NON_OFFLOAD) argument 135 #define V_ULP_MODE(x) ((x) << S_ULP_MODE) argument [all …]
|
H A D | t4_tcb.h | 13 #define V_TCB_SMAC_SEL(x) ((x) << S_TCB_SMAC_SEL) argument 22 #define V_TCB_RSS_INFO(x) ((x) << S_TCB_RSS_INFO) argument 28 #define V_TCB_TIMESTAMP(x) ((x) << S_TCB_TIMESTAMP) argument 34 #define V_TCB_T_RTT_TS_RECENT_AGE(x) ((x) << S_TCB_T_RTT_TS_RECENT_AGE) argument 39 #define V_TCB_T_RTSEQ_RECENT(x) ((x) << S_TCB_T_RTSEQ_RECENT) argument
|
H A D | t4_hw.h | 69 #define V_RSPD_NEWBUF(x) ((x) << S_RSPD_NEWBUF) argument 74 #define V_RSPD_LEN(x) ((x) << S_RSPD_LEN) argument 75 #define G_RSPD_LEN(x) (((x) >> S_RSPD_LEN) & M_RSPD_LEN) argument 78 #define V_RSPD_GEN(x) ((x) << S_RSPD_GEN) argument 83 #define V_RSPD_TYPE(x) ((x) << S_RSPD_TYPE) argument 84 #define G_RSPD_TYPE(x) (((x) >> S_RSPD_TYPE) & M_RSPD_TYPE) argument 88 #define V_QINTR_CNT_EN(x) ((x) << S_QINTR_CNT_EN) argument 93 #define V_QINTR_TIMER_IDX(x) ((x) << S_QINTR_TIMER_IDX) argument 94 #define G_QINTR_TIMER_IDX(x) (((x) >> S_QINTR_TIMER_IDX) & M_QINTR_TIMER_IDX) argument
|
H A D | t4_regs_values.h | 75 #define V_CONMCTXT_CNGTPMODE(x) ((x) << S_CONMCTXT_CNGTPMODE) argument 76 #define G_CONMCTXT_CNGTPMODE(x) \ argument 80 #define V_CONMCTXT_CNGCHMAP(x) ((x) << S_CONMCTXT_CNGCHMAP) argument 81 #define G_CONMCTXT_CNGCHMAP(x) \ argument 152 #define V_FT_VLAN_VLD(x) ((x) << S_FT_VLAN_VLD) argument
|
/dpdk/drivers/event/cnxk/ |
H A D | cnxk_eventdev_dp.h | 24 #define CNXK_TT_FROM_TAG(x) (((x) >> 32) & SSO_TT_EMPTY) argument 25 #define CNXK_TT_FROM_EVENT(x) (((x) >> 38) & SSO_TT_EMPTY) argument 26 #define CNXK_EVENT_TYPE_FROM_TAG(x) (((x) >> 28) & 0xf) argument 27 #define CNXK_SUB_EVENT_FROM_TAG(x) (((x) >> 20) & 0xff) argument 28 #define CNXK_CLR_SUB_EVENT(x) (~(0xffull << 20) & x) argument 29 #define CNXK_GRP_FROM_TAG(x) (((x) >> 36) & 0x3ff) argument 30 #define CNXK_SWTAG_PEND(x) (BIT_ULL(62) & x) argument 31 #define CNXK_TAG_IS_HEAD(x) (BIT_ULL(35) & x) argument
|
/dpdk/drivers/net/qede/base/ |
H A D | ecore_utils.h | 14 #define PTR_LO(x) ((u32)(((osal_uintptr_t)(x)) & 0xffffffff)) argument 15 #define PTR_HI(x) ((u32)((((osal_uintptr_t)(x)) >> 16) >> 16)) argument 17 #define DMA_LO(x) ((u32)(((dma_addr_t)(x)) & 0xffffffff)) argument 18 #define DMA_HI(x) ((u32)(((dma_addr_t)(x)) >> 32)) argument 20 #define DMA_LO_LE(x) OSAL_CPU_TO_LE32(DMA_LO(x)) argument 21 #define DMA_HI_LE(x) OSAL_CPU_TO_LE32(DMA_HI(x)) argument 26 #define DMA_REGPAIR_LE(x, val) (x).hi = DMA_HI_LE((val)); \ argument
|
/dpdk/drivers/common/dpaax/caamflib/ |
H A D | compat.h | 73 #define ARRAY_SIZE(x) (sizeof(x) / sizeof((x)[0])) argument 77 #define ALIGN(x, a) (((x) + ((__typeof__(x))(a) - 1)) & \ argument 103 #define swab16(x) rte_bswap16(x) argument 104 #define swab32(x) rte_bswap32(x) argument 105 #define swab64(x) rte_bswap64(x) argument 109 #define cpu_to_be32(x) (x) argument 111 #define cpu_to_be32(x) swab32(x) argument 117 #define cpu_to_le32(x) swab32(x) argument 119 #define cpu_to_le32(x) (x) argument
|
/dpdk/lib/eal/include/generic/ |
H A D | rte_byteorder.h | 126 rte_constant_bswap16(uint16_t x) rte_constant_bswap16() argument 138 rte_constant_bswap32(uint32_t x) rte_constant_bswap32() argument 150 rte_constant_bswap64(uint64_t x) rte_constant_bswap64() argument 240 rte_bswap16(x) global() argument 242 rte_bswap32(x) global() argument 244 rte_bswap64(x) global() argument 246 rte_bswap16(x) global() argument 248 rte_bswap32(x) global() argument 250 rte_bswap64(x) global() argument [all...] |
H A D | rte_rwlock.h | 96 int32_t x; in rte_rwlock_read_lock() local 133 int32_t x; in rte_rwlock_read_trylock() local 184 int32_t x; in rte_rwlock_write_trylock() local 206 int32_t x; rte_rwlock_write_lock() local [all...] |
/dpdk/drivers/net/bnxt/tf_core/ |
H A D | tf_util.h | 11 #define TF_BITS2BYTES(x) (((x) + 7) >> 3) argument 12 #define TF_BITS2BYTES_WORD_ALIGN(x) ((((x) + 31) >> 5) * 4) argument 13 #define TF_BITS2BYTES_64B_WORD_ALIGN(x) ((((x) + 63) >> 6) * 8) argument
|
/dpdk/lib/acl/ |
H A D | acl_run_avx512x8.h | 21 #define _SC_(x) ymm_##x argument 22 #define _SV_(x) (ymm_##x.y) argument 25 #define _F_(x) x##_avx512x8 argument 33 #define _M_I_(x) _mm256_##x argument 36 #define _M_SI_(x) _mm256_##x##_si256 argument 39 #define _M_MGI_(x) _mm256_m##x argument
|
H A D | acl_run_avx512x16.h | 21 #define _SC_(x) zmm_##x argument 22 #define _SV_(x) (zmm_##x.z) argument 25 #define _F_(x) x##_avx512x16 argument 33 #define _M_I_(x) _mm512_##x argument 36 #define _M_SI_(x) _mm512_##x##_si512 argument 39 #define _M_MGI_(x) _mm512_##x argument
|
/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 37 #define dev_debug(x, fmt, ...) \ argument 40 #define CXGBE_DEBUG_MBOX(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 170 #define DELAY(x) rte_delay_us(x) argument [all …]
|
/dpdk/drivers/event/dlb2/pf/base/ |
H A D | dlb2_regs.h | 11 #define DLB2_PF_VF2PF_MAILBOX(vf_id, x) \ argument 106 #define DLB2_PF_PF2VF_MAILBOX(vf_id, x) \ argument 191 #define DLB2_MSIX_VECTOR_CTRL(x) \ argument 200 #define DLB2_IOSF_FUNC_VF_BAR_DSBL(x) \ argument 294 #define DLB2_SYS_VF_LDB_VPP_V(x) \ argument 303 #define DLB2_SYS_VF_LDB_VPP2PP(x) \ argument 312 #define DLB2_SYS_VF_DIR_VPP_V(x) \ argument 321 #define DLB2_SYS_VF_DIR_VPP2PP(x) \ argument 330 #define DLB2_SYS_VF_LDB_VQID_V(x) \ argument 339 #define DLB2_SYS_VF_LDB_VQID2QID(x) \ argument [all …]
|
/dpdk/drivers/net/thunderx/base/ |
H A D | nicvf_plat.h | 24 #define nicvf_delay_us(x) rte_delay_us(x) argument 33 #define nicvf_min(x, y) RTE_MIN(x, y) argument 34 #define nicvf_log2_u32(x) rte_log2_u32(x) argument 38 #define nicvf_cpu_to_be_64(x) rte_cpu_to_be_64(x) argument 39 #define nicvf_be_to_cpu_64(x) rte_be_to_cpu_64(x) argument 50 #define ether_addr_copy(x, y) memcpy(y, x, RTE_ETHER_ADDR_LEN) argument
|
/dpdk/drivers/net/bnx2x/ |
H A D | bnx2x_ethdev.h | 43 #define DELAY(x) rte_delay_us(x) argument 44 #define DELAY_MS(x) rte_delay_ms(x) argument 45 #define usec_delay(x) DELAY(x) argument 46 #define msec_delay(x) DELAY(1000*(x)) argument
|
/dpdk/drivers/common/cnxk/ |
H A D | roc_hash.c | 29 #define F(x, y, z) (((x) & (y)) | ((~x) & (z))) argument 30 #define G(x, y, z) (((x) & (z)) | ((y) & (~z))) argument 31 #define H(x, y, z) ((x) ^ (y) ^ (z)) argument 32 #define I(x, y, z) ((y) ^ ((x) | (~z))) argument 34 #define ROTATE_LEFT(x, n) (((x) << (n)) | ((x) >> (32 - (n)))) argument 40 #define FF(a, b, c, d, x, s, ac) \ argument 47 #define GG(a, b, c, d, x, s, ac) \ argument 54 #define HH(a, b, c, d, x, s, ac) \ argument 61 #define II(a, b, c, d, x, s, ac) \ argument 80 uint32_t x[16]; in roc_hash_md5_gen() local
|
/dpdk/lib/eal/include/ |
H A D | rte_branch_prediction.h | 28 likely(x) global() argument 45 unlikely(x) global() argument [all...] |