Home
last modified time | relevance | path

Searched refs:nr (Results 1 – 25 of 31) sorted by relevance

12

/dpdk/lib/eal/include/
H A Drte_bitops.h30 #define RTE_BIT64(nr) (UINT64_C(1) << (nr)) argument
38 #define RTE_BIT32(nr) (UINT32_C(1) << (nr)) argument
59 RTE_ASSERT(nr < 32); in rte_bit_relaxed_get32()
80 RTE_ASSERT(nr < 32); in rte_bit_relaxed_set32()
101 RTE_ASSERT(nr < 32); in rte_bit_relaxed_clear32()
125 RTE_ASSERT(nr < 32); in rte_bit_relaxed_test_and_set32()
151 RTE_ASSERT(nr < 32); in rte_bit_relaxed_test_and_clear32()
178 RTE_ASSERT(nr < 64); in rte_bit_relaxed_get64()
199 RTE_ASSERT(nr < 64); in rte_bit_relaxed_set64()
220 RTE_ASSERT(nr < 64); in rte_bit_relaxed_clear64()
[all …]
/dpdk/drivers/net/ice/base/
H A Dice_bitops.h14 #define BIT_CHUNK(nr) ((nr) / BITS_PER_CHUNK) argument
18 #define BIT_IN_CHUNK(nr) ((nr) % BITS_PER_CHUNK) argument
20 #define LAST_CHUNK_BITS(nr) ((((nr) - 1) % BITS_PER_CHUNK) + 1) argument
30 return !!(*bitmap & BIT(nr)); in ice_is_bit_set_internal()
48 *bitmap &= ~BIT(nr); in ice_clear_bit_internal()
53 *bitmap |= BIT(nr); in ice_set_bit_internal()
71 ice_set_bit_internal(nr, bitmap); in ice_test_and_set_bit_internal()
86 &bitmap[BIT_CHUNK(nr)]); in ice_is_bit_set()
99 ice_clear_bit_internal(BIT_IN_CHUNK(nr), &bitmap[BIT_CHUNK(nr)]); in ice_clear_bit()
112 ice_set_bit_internal(BIT_IN_CHUNK(nr), &bitmap[BIT_CHUNK(nr)]); in ice_set_bit()
[all …]
/dpdk/drivers/common/qat/
H A Dqat_common.c30 uint32_t buf_len, nr; in qat_sgl_fill_array() local
36 for (nr = buf_len = 0; buf && nr < max_segs; buf = buf->next) { in qat_sgl_fill_array()
43 list->buffers[nr].resrvd = 0; in qat_sgl_fill_array()
57 ++nr; in qat_sgl_fill_array()
61 if (nr == max_segs) { in qat_sgl_fill_array()
69 list->num_bufs = ++nr; in qat_sgl_fill_array()
72 for (nr = 0; nr < list->num_bufs; nr++) { in qat_sgl_fill_array()
75 nr, list->buffers[nr].len, in qat_sgl_fill_array()
76 list->buffers[nr].addr); in qat_sgl_fill_array()
78 virt_addr[nr], in qat_sgl_fill_array()
[all …]
/dpdk/drivers/net/pfe/base/
H A Dpfe.h14 set_bit(unsigned long nr, void *addr) in set_bit() argument
16 int *m = ((int *)addr) + (nr >> 5); in set_bit()
17 *m |= 1 << (nr & 31); in set_bit()
21 test_bit(int nr, const void *addr) in test_bit() argument
23 return (1UL & (((const int *)addr)[nr >> 5] >> (nr & 31))) != 0UL; in test_bit()
30 clear_bit(unsigned long nr, void *addr) in clear_bit() argument
32 int *m = ((int *)addr) + (nr >> 5); in clear_bit()
33 *m &= ~(1 << (nr & 31)); in clear_bit()
43 int *m = ((int *)addr) + (nr >> 5); in test_and_clear_bit()
57 int *m = ((int *)addr) + (nr >> 5); in test_and_set_bit()
[all …]
/dpdk/drivers/common/cnxk/
H A Droc_bits.h9 #define BIT_ULL(nr) (1ULL << (nr)) argument
13 #define BIT(nr) (1UL << (nr)) argument
/dpdk/drivers/net/ionic/
H A Dionic_osdep.h24 #define BIT(nr) (1UL << (nr)) argument
25 #define BIT_ULL(nr) (1ULL << (nr)) argument
/dpdk/lib/net/
H A Drte_l2tpv2.h138 rte_be16_t nr; /**< Nr(16) */ member
151 rte_be16_t nr; /**< Nr(16) */ member
178 rte_be16_t nr; /**< Nr(16) */ member
198 rte_be16_t nr; /**< Nr(16) */ member
/dpdk/drivers/net/hns3/
H A Dhns3_ethdev.h946 #define BIT(nr) (1UL << (nr)) argument
1010 hns3_atomic_test_bit(unsigned int nr, volatile uint64_t *addr) in hns3_atomic_test_bit() argument
1014 res = (__atomic_load_n(addr, __ATOMIC_RELAXED) & (1UL << nr)) != 0; in hns3_atomic_test_bit()
1019 hns3_atomic_set_bit(unsigned int nr, volatile uint64_t *addr) in hns3_atomic_set_bit() argument
1021 __atomic_fetch_or(addr, (1UL << nr), __ATOMIC_RELAXED); in hns3_atomic_set_bit()
1025 hns3_atomic_clear_bit(unsigned int nr, volatile uint64_t *addr) in hns3_atomic_clear_bit() argument
1027 __atomic_fetch_and(addr, ~(1UL << nr), __ATOMIC_RELAXED); in hns3_atomic_clear_bit()
1031 hns3_test_and_clear_bit(unsigned int nr, volatile uint64_t *addr) in hns3_test_and_clear_bit() argument
1033 uint64_t mask = (1UL << nr); in hns3_test_and_clear_bit()
/dpdk/drivers/crypto/bcmfs/
H A Dbcmfs_hw_defs.h15 #define BIT(nr) (1UL << (nr)) argument
/dpdk/app/test/
H A Dtest_ring_stress_impl.h279 uint32_t i, nr; in mt1_init() local
298 nr = 2 * num; in mt1_init()
299 sz = rte_ring_get_memsize(nr); in mt1_init()
303 __func__, sz, nr); in mt1_init()
309 rc = _st_ring_init(r, RING_NAME, nr); in mt1_init()
312 __func__, r, nr, rc, strerror(-rc)); in mt1_init()
/dpdk/drivers/common/dpaax/caamflib/
H A Dcompat.h80 #define BIT(nr) (1UL << (nr)) argument
/dpdk/drivers/net/enic/base/
H A Dvnic_devcmd.h50 #define _CMDCF(dir, flags, vtype, nr) \ argument
54 ((nr) << _CMD_NSHIFT))
55 #define _CMDC(dir, vtype, nr) _CMDCF(dir, 0, vtype, nr) argument
56 #define _CMDCNW(dir, vtype, nr) _CMDCF(dir, _CMD_FLAGS_NOWAIT, vtype, nr) argument
/dpdk/lib/acl/
H A Dacl_run_avx512.c78 xmm_t cp, cr, np, nr; in resolve_mcle8_avx512x1() local
97 nr = _mm_loadu_si128((const xmm_t *)(res + mn)); in resolve_mcle8_avx512x1()
101 cr = _mm_mask_mov_epi32(nr, msk, cr); in resolve_mcle8_avx512x1()
H A Dacl_run_avx512x16.h253 __m512i cp, cr, np, nr; in resolve_mcgt8_avx512x1() local
272 nr = _mm512_maskz_loadu_epi32(cm, res + mi); in resolve_mcgt8_avx512x1()
276 cr = _mm512_mask_mov_epi32(nr, sm, cr); in resolve_mcgt8_avx512x1()
H A Dacl_run_avx512_common.h411 _T_simd cp, cr, np, nr, mch; in _F_() local
433 nr = _M_MGI_(mask_i32gather_epi32)(zero, msk, mch, res, in _F_()
439 cr = _M_I_(mask_mov_epi32)(nr, m, cr); in _F_()
/dpdk/drivers/dma/dpaa/
H A Ddpaa_qdma.h11 #define BIT(nr) (1UL << (nr)) argument
/dpdk/drivers/crypto/ccp/
H A Dccp_dev.h138 #define CCP_BITMAP_SIZE(nr) \ argument
139 CCP_DIV_ROUND_UP(nr, CHAR_BIT * sizeof(unsigned long))
H A Dccp_dev.c261 unsigned int nr) in ccp_bitmap_find_next_zero_area() argument
268 end = index + nr; in ccp_bitmap_find_next_zero_area()
/dpdk/drivers/net/softnic/
H A Drte_eth_softnic_tm.c2493 struct tm_node *nr = tm_root_node_present(dev), *ns, *np, *nt, *nq; in hierarchy_commit_check() local
2499 if (nr == NULL) in hierarchy_commit_check()
2507 if (nr->n_children == 0 || nr->n_children > TM_MAX_SUBPORTS) in hierarchy_commit_check()
3247 struct tm_node *nr, in read_port_stats() argument
3271 nr->stats.n_pkts += in read_port_stats()
3273 nr->stats.n_bytes += in read_port_stats()
3275 nr->stats.leaf.n_pkts_dropped[RTE_COLOR_GREEN] += in read_port_stats()
3277 nr->stats.leaf.n_bytes_dropped[RTE_COLOR_GREEN] += in read_port_stats()
3284 memcpy(stats, &nr->stats, sizeof(*stats)); in read_port_stats()
3291 memset(&nr->stats, 0, sizeof(nr->stats)); in read_port_stats()
/dpdk/drivers/net/ena/base/
H A Dena_plat_dpdk.h109 #define BIT(nr) (1UL << (nr)) argument
/dpdk/app/test-fib/
H A Dmain.c175 uint32_t nr = 0; in complete_distrib() local
191 nr += config.nb_routes_per_depth[depth]; in complete_distrib()
196 if (nr > n) { in complete_distrib()
207 uint32_t avg_routes_left = (n - nr) / in complete_distrib()
211 nr += config.nb_routes_per_depth[depth]; in complete_distrib()
/dpdk/drivers/net/octeontx/
H A Docteontx_rxtx.h14 #define BIT(nr) (1UL << (nr)) argument
/dpdk/drivers/net/qede/base/
H A Dbcm_osal.h314 #define OSAL_BIT(nr) (1UL << (nr)) argument
/dpdk/drivers/net/bnx2x/
H A Dbnx2x.h1537 #define BNX2X_FP(sc, nr, var) ((sc)->fp[(nr)].var) argument
1540 #define bnx2x_fp(sc, nr, var) ((sc)->fp[nr].var) argument
/dpdk/doc/guides/howto/
H A Dpacket_capture_framework.rst102 $ tcpdump -nr /tmp/capture.pcapng

12