Home
last modified time | relevance | path

Searched refs:fdir (Results 1 – 25 of 53) sorted by relevance

123

/dpdk/drivers/net/i40e/
H A Di40e_fdir.c176 vsi = pf->fdir.fdir_vsi; in i40e_fdir_setup()
188 pf->fdir.fdir_vsi = vsi; in i40e_fdir_setup()
268 pf->fdir.rxq = NULL; in i40e_fdir_setup()
271 pf->fdir.txq = NULL; in i40e_fdir_setup()
274 pf->fdir.fdir_vsi = NULL; in i40e_fdir_setup()
288 vsi = pf->fdir.fdir_vsi; in i40e_fdir_teardown()
304 pf->fdir.rxq = NULL; in i40e_fdir_teardown()
306 pf->fdir.txq = NULL; in i40e_fdir_teardown()
308 pf->fdir.fdir_vsi = NULL; in i40e_fdir_teardown()
2195 fdir->guarant_spc = in i40e_fdir_info_get()
[all …]
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()
439 const __m256i fdir = _mm256_slli_epi32(rss_fdir_bits, 28); in _recv_raw_pkts_vec_avx2() local
448 const __m256i fdir_mask = _mm256_cmpeq_epi32(fdir, fdir_id); in _recv_raw_pkts_vec_avx2()
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()
[all …]
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()
567 const __m256i fdir = in _recv_raw_pkts_vec_avx512() local
578 _mm256_cmpeq_epi32(fdir, fdir_id); in _recv_raw_pkts_vec_avx512()
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()
[all …]
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.c232 mb->hash.fdir.hi = in i40e_rxd_build_fdir()
236 mb->hash.fdir.hi = in i40e_rxd_build_fdir()
241 mb->hash.fdir.lo = in i40e_rxd_build_fdir()
246 mb->hash.fdir.hi = in i40e_rxd_build_fdir()
3086 txq->reg_idx = pf->fdir.fdir_vsi->base_queue; in i40e_fdir_setup_tx_resources()
3087 txq->vsi = pf->fdir.fdir_vsi; in i40e_fdir_setup_tx_resources()
3097 pf->fdir.txq = txq; in i40e_fdir_setup_tx_resources()
3098 pf->fdir.txq_available_buf_count = I40E_FDIR_PRG_PKT_CNT; in i40e_fdir_setup_tx_resources()
3145 rxq->reg_idx = pf->fdir.fdir_vsi->base_queue; in i40e_fdir_setup_rx_resources()
3146 rxq->vsi = pf->fdir.fdir_vsi; in i40e_fdir_setup_rx_resources()
[all …]
H A Di40e_flow.c3295 if (pf->fdir.fdir_vsi == NULL) { in i40e_flow_parse_fdir_filter()
3314 if (TAILQ_EMPTY(&pf->fdir.fdir_list)) in i40e_flow_parse_fdir_filter()
4638 struct i40e_fdir_info *fdir_info = &pf->fdir; in i40e_flow_create()
4678 flow->rule = TAILQ_LAST(&pf->fdir.fdir_list, in i40e_flow_create()
4724 struct i40e_fdir_info *fdir_info = &pf->fdir; in i40e_flow_destroy()
4742 if (!ret && TAILQ_EMPTY(&pf->fdir.fdir_list)) { in i40e_flow_destroy()
4907 struct i40e_fdir_info *fdir_info = &pf->fdir; in i40e_flow_flush_fdir_filter()
4920 &fdir_filter->fdir.input); in i40e_flow_flush_fdir_filter()
4949 pf->fdir.flow_count[pctype] = 0; in i40e_flow_flush_fdir_filter()
4950 pf->fdir.flex_mask_flag[pctype] = 0; in i40e_flow_flush_fdir_filter()
[all …]
/dpdk/app/test/
H A Dprocess.h72 int fd, fdir; in process_dup() local
85 fdir = dirfd(dir); in process_dup()
86 if (fdir < 0) { in process_dup()
90 fdir, procdir, in process_dup()
108 if (fd == fdir || fd <= 2) in process_dup()
/dpdk/drivers/net/hns3/
H A Dhns3_fdir.c314 switch (pf->fdir.fd_cfg.fd_mode) { in hns3_init_fd_config()
324 pf->fdir.fd_cfg.fd_mode); in hns3_init_fd_config()
372 pf->fdir.fd_cfg.rule_num[HNS3_FD_STAGE_1], in hns3_init_fd_config()
373 pf->fdir.fd_cfg.cnt_num[HNS3_FD_STAGE_1], in hns3_init_fd_config()
374 pf->fdir.fd_cfg.rule_num[HNS3_FD_STAGE_2], in hns3_init_fd_config()
375 pf->fdir.fd_cfg.cnt_num[HNS3_FD_STAGE_2]); in hns3_init_fd_config()
826 struct hns3_fdir_info *fdir_info = &pf->fdir; in hns3_fdir_filter_init()
868 struct hns3_fdir_info *fdir_info = &pf->fdir; in hns3_fdir_filter_uninit()
960 struct hns3_fdir_info *fdir_info = &pf->fdir; in hns3_fdir_filter_program()
1025 struct hns3_fdir_info *fdir_info = &pf->fdir; in hns3_clear_all_fdir_filter()
[all …]
/dpdk/drivers/net/ice/
H A Dice_fdir_filter.c455 if (pf->fdir.fdir_vsi) { in ice_fdir_setup()
466 pf->fdir.fdir_vsi = vsi; in ice_fdir_setup()
524 pf->fdir.mz = mz; in ice_fdir_setup()
540 pf->fdir.mz = NULL; in ice_fdir_setup()
543 pf->fdir.rxq = NULL; in ice_fdir_setup()
546 pf->fdir.txq = NULL; in ice_fdir_setup()
631 vsi = pf->fdir.fdir_vsi; in ice_fdir_teardown()
652 pf->fdir.txq = NULL; in ice_fdir_teardown()
654 pf->fdir.rxq = NULL; in ice_fdir_teardown()
660 if (pf->fdir.mz) { in ice_fdir_teardown()
[all …]
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_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()
H A Dice_rxtx.c809 rxq = pf->fdir.rxq; in ice_fdir_rx_queue_start()
852 txq = pf->fdir.txq; in ice_fdir_tx_queue_start()
1012 rxq = pf->fdir.rxq; in ice_fdir_rx_queue_stop()
1037 txq = pf->fdir.txq; in ice_fdir_tx_queue_stop()
2262 txq->reg_idx = pf->fdir.fdir_vsi->base_queue; in ice_fdir_setup_tx_resources()
2263 txq->vsi = pf->fdir.fdir_vsi; in ice_fdir_setup_tx_resources()
2272 pf->fdir.txq = txq; in ice_fdir_setup_tx_resources()
2322 rxq->vsi = pf->fdir.fdir_vsi; in ice_fdir_setup_rx_resources()
2334 pf->fdir.rxq = rxq; in ice_fdir_setup_rx_resources()
4304 struct ice_tx_queue *txq = pf->fdir.txq; in ice_fdir_programming()
[all …]
/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/app/test-pmd/
H A Dutil.c169 "ID=0x%x", mb->hash.fdir.hi); in dump_pkt_burst()
173 mb->hash.fdir.hi, mb->hash.fdir.lo); in dump_pkt_burst()
177 mb->hash.fdir.hash, mb->hash.fdir.id); in dump_pkt_burst()
/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()
H A Diavf_rxtx_vec_avx512.c1106 rx_pkts[i + 0]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1109 rx_pkts[i + 1]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1112 rx_pkts[i + 2]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1115 rx_pkts[i + 3]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1118 rx_pkts[i + 4]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1121 rx_pkts[i + 5]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1124 rx_pkts[i + 6]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1127 rx_pkts[i + 7]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
H A Diavf_rxtx_vec_sse.c306 rx_pkts[0]->hash.fdir.hi = in flex_desc_to_olflags_v()
309 rx_pkts[1]->hash.fdir.hi = in flex_desc_to_olflags_v()
312 rx_pkts[2]->hash.fdir.hi = in flex_desc_to_olflags_v()
315 rx_pkts[3]->hash.fdir.hi = in flex_desc_to_olflags_v()
/dpdk/drivers/net/bnxt/
H A Dbnxt_rxr.c271 mbuf->hash.fdir.id = tpa_info->cfa_code; in bnxt_tpa_start()
807 mbuf->hash.fdir.hi = mark_id; in bnxt_ulp_set_mark_in_mbuf()
809 mbuf->hash.fdir.id = rxcmp1->cfa_code; in bnxt_ulp_set_mark_in_mbuf()
815 mbuf->hash.fdir.hi = 0; in bnxt_ulp_set_mark_in_mbuf()
816 mbuf->hash.fdir.id = 0; in bnxt_ulp_set_mark_in_mbuf()
837 mbuf->hash.fdir.hi = bp->mark_table[cfa_code].mark_id; in bnxt_set_mark_in_mbuf()
/dpdk/drivers/net/enic/
H A Denic_rxtx_common.h233 mbuf->hash.fdir.hi = filter_id - 1; in enic_cq_rx_to_pkt_flags()
/dpdk/drivers/net/qede/
H A Dqede_filter.c147 struct rte_eth_fdir_conf *fdir = &eth_dev->data->dev_conf.fdir_conf; in qede_check_fdir_support() local
150 switch (fdir->mode) { in qede_check_fdir_support()
169 DP_ERR(edev, "Unsupported flowdir mode %d\n", fdir->mode); in qede_check_fdir_support()
/dpdk/drivers/net/txgbe/
H A Dtxgbe_ethdev.h349 struct txgbe_hw_fdir_info fdir; member
386 (&((struct txgbe_adapter *)(dev)->data->dev_private)->fdir)

123