Home
last modified time | relevance | path

Searched refs:hi (Results 1 – 25 of 81) sorted by relevance

1234

/dpdk/drivers/net/qede/base/
H A Decore_utils.h26 #define DMA_REGPAIR_LE(x, val) (x).hi = DMA_HI_LE((val)); \
29 #define HILO_GEN(hi, lo, type) ((((type)(hi)) << 32) + (lo)) argument
30 #define HILO_DMA(hi, lo) HILO_GEN(hi, lo, dma_addr_t) argument
31 #define HILO_64(hi, lo) HILO_GEN(hi, lo, u64) argument
32 #define HILO_DMA_REGPAIR(regpair) (HILO_DMA(regpair.hi, regpair.lo))
33 #define HILO_64_REGPAIR(regpair) (HILO_64(regpair.hi, regpair.lo))
/dpdk/lib/eal/linux/
H A Deal_memalloc.c535 alloc_sz = hi->hugepage_sz; in alloc_seg()
805 struct hugepage_info *hi; member
945 struct hugepage_info *hi; member
1022 struct hugepage_info *hi = NULL; in eal_memalloc_alloc_seg_bulk() local
1039 if (!hi) { in eal_memalloc_alloc_seg_bulk()
1054 wa.hi = hi; in eal_memalloc_alloc_seg_bulk()
1127 wa.hi = hi; in eal_memalloc_free_seg_bulk()
1215 p_ms->socket_id, hi, in sync_chunk()
1348 hi->hugedir, strerror(errno)); in sync_existing()
1354 hi->hugedir, strerror(errno)); in sync_existing()
[all …]
/dpdk/lib/eal/windows/
H A Deal_memalloc.c36 struct hugepage_info *hi) in alloc_seg() argument
63 alloc_sz = hi->hugepage_sz; in alloc_seg()
129 ms->hugepage_sz = hi->hugepage_sz; in alloc_seg()
169 struct hugepage_info *hi; member
276 struct hugepage_info *hi; member
316 struct hugepage_info *hi = NULL; in eal_memalloc_alloc_seg_bulk() local
328 hi = hpi; in eal_memalloc_alloc_seg_bulk()
332 if (!hi) { in eal_memalloc_alloc_seg_bulk()
339 wa.hi = hi; in eal_memalloc_alloc_seg_bulk()
379 struct hugepage_info *hi = NULL; in eal_memalloc_free_seg_bulk() local
[all …]
/dpdk/drivers/net/txgbe/
H A Dtxgbe_rxtx.h26 } hi; member
41 } hi; member
82 #define TXGBE_RXD_IPID(rxd) ((rxd)->qw0.hi.ipid)
83 #define TXGBE_RXD_CSUM(rxd) ((rxd)->qw0.hi.csum)
86 #define TXGBE_RXD_FDIRID(rxd) ((rxd)->qw0.hi.dw1)
145 #define TXGBE_RXD_LENGTH(rxd) ((rxd)->qw1.hi.len)
146 #define TXGBE_RXD_VLAN(rxd) ((rxd)->qw1.hi.tag)
/dpdk/drivers/net/ngbe/
H A Dngbe_rxtx.h26 } hi; member
41 } hi; member
81 #define NGBE_RXD_IPID(rxd) ((rxd)->qw0.hi.ipid)
82 #define NGBE_RXD_CSUM(rxd) ((rxd)->qw0.hi.csum)
122 #define NGBE_RXD_LENGTH(rxd) ((rxd)->qw1.hi.len)
123 #define NGBE_RXD_VLAN(rxd) ((rxd)->qw1.hi.tag)
/dpdk/lib/acl/
H A Dacl_vect.h21 #define ACL_TR_HILO(P, TC, tr0, tr1, lo, hi) do { \ argument
23 hi = (typeof(hi))_##P##_shuffle_ps((TC)(tr0), (TC)(tr1), 0xdd); \
H A Dacl_bld.c803 acl_add_ptr_range(context, root, node, lo, hi); in acl_gen_range_mdl()
841 acl_add_ptr_range(context, root, end, 0, hi[0]); in acl_gen_range_high()
846 acl_add_ptr_range(context, root, node, hi[n], hi[n]); in acl_gen_range_high()
849 acl_gen_range_high(context, node, end, hi, n, level); in acl_gen_range_high()
852 if (n > 1 && hi[n - 1] != 0) in acl_gen_range_high()
866 const uint8_t *hi; in acl_gen_range_trie() local
869 hi = max; in acl_gen_range_trie()
876 for (n = size - 1; n > 0 && lo[n] == hi[n]; n--) { in acl_gen_range_trie()
878 acl_add_ptr_range(context, prev, node, lo[n], hi[n]); in acl_gen_range_trie()
892 hi_ff &= hi[k]; in acl_gen_range_trie()
[all …]
H A Dacl_run_avx2.h95 ymm_t lo, hi; in acl_process_matches_avx2x8() local
126 ACL_TR_HILO(mm256, __m256, t0, t1, lo, hi); in acl_process_matches_avx2x8()
130 *tr_hi = _mm256_blendv_epi8(*tr_hi, hi, matches); in acl_process_matches_avx2x8()
/dpdk/drivers/net/cxgbe/
H A Dclip_tbl.c16 u64 hi = ((u64)lip[1]) << 32 | lip[0]; in clip6_get_mbox() local
23 c.ip_hi = hi; in clip6_get_mbox()
35 u64 hi = ((u64)lip[1]) << 32 | lip[0]; in clip6_release_mbox() local
42 c.ip_hi = hi; in clip6_release_mbox()
/dpdk/drivers/bus/dpaa/include/
H A Dfsl_bman.h48 u16 hi; /* High 16-bits of 48-bit address */ member
52 u16 hi;
82 __buf931->hi = upper_32_bits(v); \
/dpdk/drivers/net/i40e/
H A Di40e_rxtx_vec_avx2.c71 rx_pkts[idx_0]->hash.fdir.hi = _mm256_extract_epi32(desc_fdir_data, 0); in desc_fdir_processing_32b()
72 rx_pkts[idx_1]->hash.fdir.hi = _mm256_extract_epi32(desc_fdir_data, 4); in desc_fdir_processing_32b()
465 rx_pkts[i + 0]->hash.fdir.hi = _mm256_extract_epi32(fdir_mb0_1, 3); in _recv_raw_pkts_vec_avx2()
466 rx_pkts[i + 1]->hash.fdir.hi = _mm256_extract_epi32(fdir_mb0_1, 7); in _recv_raw_pkts_vec_avx2()
476 rx_pkts[i + 2]->hash.fdir.hi = _mm256_extract_epi32(fdir_mb2_3, 3); in _recv_raw_pkts_vec_avx2()
477 rx_pkts[i + 3]->hash.fdir.hi = _mm256_extract_epi32(fdir_mb2_3, 7); in _recv_raw_pkts_vec_avx2()
484 rx_pkts[i + 4]->hash.fdir.hi = _mm256_extract_epi32(fdir_mb4_5, 3); in _recv_raw_pkts_vec_avx2()
485 rx_pkts[i + 5]->hash.fdir.hi = _mm256_extract_epi32(fdir_mb4_5, 7); in _recv_raw_pkts_vec_avx2()
492 rx_pkts[i + 6]->hash.fdir.hi = _mm256_extract_epi32(fdir_mb6_7, 3); in _recv_raw_pkts_vec_avx2()
493 rx_pkts[i + 7]->hash.fdir.hi = _mm256_extract_epi32(fdir_mb6_7, 7); in _recv_raw_pkts_vec_avx2()
H A Di40e_rxtx_vec_sse.c137 rx_pkt[0]->hash.fdir.hi = _mm_extract_epi32(v_fdir_ids, 0); in descs_to_fdir_32b()
138 rx_pkt[1]->hash.fdir.hi = _mm_extract_epi32(v_fdir_ids, 1); in descs_to_fdir_32b()
139 rx_pkt[2]->hash.fdir.hi = _mm_extract_epi32(v_fdir_ids, 2); in descs_to_fdir_32b()
140 rx_pkt[3]->hash.fdir.hi = _mm_extract_epi32(v_fdir_ids, 3); in descs_to_fdir_32b()
184 rx_pkt[0]->hash.fdir.hi = _mm_extract_epi32(v_fdir_ids, 0); in descs_to_fdir_16b()
185 rx_pkt[1]->hash.fdir.hi = _mm_extract_epi32(v_fdir_ids, 1); in descs_to_fdir_16b()
186 rx_pkt[2]->hash.fdir.hi = _mm_extract_epi32(v_fdir_ids, 2); in descs_to_fdir_16b()
187 rx_pkt[3]->hash.fdir.hi = _mm_extract_epi32(v_fdir_ids, 3); in descs_to_fdir_16b()
H A Di40e_rxtx_vec_neon.c125 rx_pkt[0]->hash.fdir.hi = vgetq_lane_u32(v_fdir_ids, 0); in descs_to_fdir_32b()
126 rx_pkt[1]->hash.fdir.hi = vgetq_lane_u32(v_fdir_ids, 1); in descs_to_fdir_32b()
127 rx_pkt[2]->hash.fdir.hi = vgetq_lane_u32(v_fdir_ids, 2); in descs_to_fdir_32b()
128 rx_pkt[3]->hash.fdir.hi = vgetq_lane_u32(v_fdir_ids, 3); in descs_to_fdir_32b()
168 rx_pkt[0]->hash.fdir.hi = vgetq_lane_u32(v_fdir_ids, 0); in descs_to_fdir_16b()
169 rx_pkt[1]->hash.fdir.hi = vgetq_lane_u32(v_fdir_ids, 1); in descs_to_fdir_16b()
170 rx_pkt[2]->hash.fdir.hi = vgetq_lane_u32(v_fdir_ids, 2); in descs_to_fdir_16b()
171 rx_pkt[3]->hash.fdir.hi = vgetq_lane_u32(v_fdir_ids, 3); in descs_to_fdir_16b()
H A Di40e_rxtx_vec_avx512.c197 rx_pkts[idx_0]->hash.fdir.hi = _mm256_extract_epi32(desc_fdir_data, 0); in desc_fdir_processing_32b()
198 rx_pkts[idx_1]->hash.fdir.hi = _mm256_extract_epi32(desc_fdir_data, 4); in desc_fdir_processing_32b()
598 rx_pkts[i + 0]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
600 rx_pkts[i + 1]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
613 rx_pkts[i + 2]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
615 rx_pkts[i + 3]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
625 rx_pkts[i + 4]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
627 rx_pkts[i + 5]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
637 rx_pkts[i + 6]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
639 rx_pkts[i + 7]->hash.fdir.hi = in _recv_raw_pkts_vec_avx512()
/dpdk/drivers/net/mlx5/
H A Dmlx5_rxtx_vec_neon.h204 const uint32_t flow_tag = t_pkt->hash.fdir.hi; in rxq_cq_decompress_v()
207 elts[pos]->hash.fdir.hi = flow_tag; in rxq_cq_decompress_v()
208 elts[pos + 1]->hash.fdir.hi = flow_tag; in rxq_cq_decompress_v()
209 elts[pos + 2]->hash.fdir.hi = flow_tag; in rxq_cq_decompress_v()
210 elts[pos + 3]->hash.fdir.hi = flow_tag; in rxq_cq_decompress_v()
254 elts[pos]->hash.fdir.hi = in rxq_cq_decompress_v()
256 elts[pos + 1]->hash.fdir.hi = in rxq_cq_decompress_v()
258 elts[pos + 2]->hash.fdir.hi = in rxq_cq_decompress_v()
260 elts[pos + 3]->hash.fdir.hi = in rxq_cq_decompress_v()
H A Dmlx5_rxtx_vec_sse.h189 const uint32_t flow_tag = t_pkt->hash.fdir.hi; in rxq_cq_decompress_v()
192 elts[pos]->hash.fdir.hi = flow_tag; in rxq_cq_decompress_v()
193 elts[pos + 1]->hash.fdir.hi = flow_tag; in rxq_cq_decompress_v()
194 elts[pos + 2]->hash.fdir.hi = flow_tag; in rxq_cq_decompress_v()
195 elts[pos + 3]->hash.fdir.hi = flow_tag; in rxq_cq_decompress_v()
239 elts[pos]->hash.fdir.hi = in rxq_cq_decompress_v()
241 elts[pos + 1]->hash.fdir.hi = in rxq_cq_decompress_v()
243 elts[pos + 2]->hash.fdir.hi = in rxq_cq_decompress_v()
245 elts[pos + 3]->hash.fdir.hi = in rxq_cq_decompress_v()
H A Dmlx5_rxtx_vec_altivec.h260 const uint32_t flow_tag = t_pkt->hash.fdir.hi; in rxq_cq_decompress_v()
263 elts[pos]->hash.fdir.hi = flow_tag; in rxq_cq_decompress_v()
264 elts[pos + 1]->hash.fdir.hi = flow_tag; in rxq_cq_decompress_v()
265 elts[pos + 2]->hash.fdir.hi = flow_tag; in rxq_cq_decompress_v()
266 elts[pos + 3]->hash.fdir.hi = flow_tag; in rxq_cq_decompress_v()
353 elts[pos]->hash.fdir.hi = in rxq_cq_decompress_v()
355 elts[pos + 1]->hash.fdir.hi = in rxq_cq_decompress_v()
357 elts[pos + 2]->hash.fdir.hi = in rxq_cq_decompress_v()
359 elts[pos + 3]->hash.fdir.hi = in rxq_cq_decompress_v()
/dpdk/drivers/net/ice/
H A Dice_rxtx_vec_avx2.c445 rx_pkts[i + 0]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
448 rx_pkts[i + 1]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
451 rx_pkts[i + 2]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
454 rx_pkts[i + 3]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
457 rx_pkts[i + 4]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
460 rx_pkts[i + 5]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
463 rx_pkts[i + 6]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
466 rx_pkts[i + 7]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
H A Dice_rxtx.h331 uint32_t hi, lo, lo2, delta; in ice_tstamp_convert_32b_64b() local
336 hi = ICE_READ_REG(hw, GLTSYN_TIME_H(0)); in ice_tstamp_convert_32b_64b()
349 hi = ICE_READ_REG(hw, GLTSYN_TIME_H(0)); in ice_tstamp_convert_32b_64b()
352 ad->time_hw = ((uint64_t)hi << 32) | lo; in ice_tstamp_convert_32b_64b()
H A Dice_rxtx_vec_avx512.c556 rx_pkts[i + 0]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
559 rx_pkts[i + 1]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
562 rx_pkts[i + 2]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
565 rx_pkts[i + 3]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
568 rx_pkts[i + 4]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
571 rx_pkts[i + 5]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
574 rx_pkts[i + 6]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
577 rx_pkts[i + 7]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
H A Dice_rxtx_vec_sse.c234 rx_pkts[0]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
237 rx_pkts[1]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
240 rx_pkts[2]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
243 rx_pkts[3]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
/dpdk/lib/ethdev/
H A Dethdev_private.c76 uint16_t lo, hi, val; in rte_eth_devargs_process_range() local
80 result = sscanf(str, "%hu%n-%hu%n", &lo, &n, &hi, &n); in rte_eth_devargs_process_range()
85 if (lo > hi) in rte_eth_devargs_process_range()
87 for (val = lo; val <= hi; val++) { in rte_eth_devargs_process_range()
/dpdk/drivers/net/bnx2x/
H A Dbnx2x_stats.h452 DIFF_64(diff.hi, new->s##_hi, pstats->mac_stx[0].t##_hi, \
456 ADD_64(pstats->mac_stx[1].t##_hi, diff.hi, \
462 DIFF_64(diff.hi, new->s##_hi, old->s##_hi, \
464 ADD_64(estats->t##_hi, diff.hi, \
526 qstats->t##_hi = qstats_old->t##_hi + le32toh(s.hi); \
/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_avx2.c879 rx_pkts[i + 0]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
882 rx_pkts[i + 1]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
885 rx_pkts[i + 2]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
888 rx_pkts[i + 3]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
891 rx_pkts[i + 4]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
894 rx_pkts[i + 5]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
897 rx_pkts[i + 6]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
900 rx_pkts[i + 7]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
/dpdk/drivers/net/ice/base/
H A Dice_ptp_hw.c93 u32 lo, hi; in ice_ptp_read_src_incval() local
99 hi = rd32(hw, GLTSYN_INCVAL_H(tmr_idx)); in ice_ptp_read_src_incval()
101 return ((u64)(hi & INCVAL_HIGH_M) << 32) | lo; in ice_ptp_read_src_incval()
639 u32 lo, hi; in ice_read_phy_tstamp_e822() local
651 status = ice_read_quad_reg_e822(hw, quad, hi_addr, &hi); in ice_read_phy_tstamp_e822()
2488 u32 lo, hi, val; in ice_start_phy_timer_e822() local
2509 hi = rd32(hw, GLTSYN_INCVAL_H(tmr_idx)); in ice_start_phy_timer_e822()
2510 incval = (u64)hi << 32 | lo; in ice_start_phy_timer_e822()
2765 u32 lo_addr, hi_addr, lo, hi; in ice_read_phy_tstamp_e810() local
2777 status = ice_read_phy_reg_e810(hw, hi_addr, &hi); in ice_read_phy_tstamp_e810()
[all …]

1234