Home
last modified time | relevance | path

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

12

/f-stack/dpdk/drivers/net/i40e/
H A Di40e_fdir.c175 vsi = pf->fdir.fdir_vsi; in i40e_fdir_setup()
187 pf->fdir.fdir_vsi = vsi; in i40e_fdir_setup()
267 pf->fdir.rxq = NULL; in i40e_fdir_setup()
270 pf->fdir.txq = NULL; in i40e_fdir_setup()
273 pf->fdir.fdir_vsi = NULL; in i40e_fdir_setup()
288 vsi = pf->fdir.fdir_vsi; in i40e_fdir_teardown()
305 pf->fdir.rxq = NULL; in i40e_fdir_teardown()
308 pf->fdir.txq = NULL; in i40e_fdir_teardown()
310 pf->fdir.fdir_vsi = NULL; in i40e_fdir_teardown()
2093 fdir->guarant_spc = in i40e_fdir_info_get()
[all …]
H A Di40e_rxtx_vec_avx2.c183 rx_pkts[idx_0]->hash.fdir.hi = _mm256_extract_epi32(desc_fdir_data, 0); in desc_fdir_processing_32b()
184 rx_pkts[idx_1]->hash.fdir.hi = _mm256_extract_epi32(desc_fdir_data, 4); in desc_fdir_processing_32b()
543 const __m256i fdir = _mm256_slli_epi32(rss_fdir_bits, 28); in _recv_raw_pkts_vec_avx2() local
552 const __m256i fdir_mask = _mm256_cmpeq_epi32(fdir, fdir_id); in _recv_raw_pkts_vec_avx2()
569 rx_pkts[i + 0]->hash.fdir.hi = _mm256_extract_epi32(fdir_mb0_1, 3); in _recv_raw_pkts_vec_avx2()
570 rx_pkts[i + 1]->hash.fdir.hi = _mm256_extract_epi32(fdir_mb0_1, 7); in _recv_raw_pkts_vec_avx2()
580 rx_pkts[i + 2]->hash.fdir.hi = _mm256_extract_epi32(fdir_mb2_3, 3); in _recv_raw_pkts_vec_avx2()
581 rx_pkts[i + 3]->hash.fdir.hi = _mm256_extract_epi32(fdir_mb2_3, 7); in _recv_raw_pkts_vec_avx2()
588 rx_pkts[i + 4]->hash.fdir.hi = _mm256_extract_epi32(fdir_mb4_5, 3); in _recv_raw_pkts_vec_avx2()
589 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_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_flow.c2264 if (pf->fdir.inset_flag[pctype] && in i40e_flow_set_fdir_inset()
2268 if (pf->fdir.inset_flag[pctype] && in i40e_flow_set_fdir_inset()
2318 pf->fdir.input_set[pctype] = input_set; in i40e_flow_set_fdir_inset()
2319 pf->fdir.inset_flag[pctype] = 1; in i40e_flow_set_fdir_inset()
3299 if (pf->fdir.fdir_vsi == NULL) { in i40e_flow_parse_fdir_filter()
3318 if (TAILQ_EMPTY(&pf->fdir.fdir_list)) in i40e_flow_parse_fdir_filter()
5198 struct i40e_fdir_info *fdir_info = &pf->fdir; in i40e_flow_create()
5238 flow->rule = TAILQ_LAST(&pf->fdir.fdir_list, in i40e_flow_create()
5485 &fdir_filter->fdir.input); in i40e_flow_flush_fdir_filter()
5514 pf->fdir.inset_flag[pctype] = 0; in i40e_flow_flush_fdir_filter()
[all …]
H A Di40e_rxtx.c192 mb->hash.fdir.hi = in i40e_rxd_build_fdir()
196 mb->hash.fdir.hi = in i40e_rxd_build_fdir()
201 mb->hash.fdir.lo = in i40e_rxd_build_fdir()
206 mb->hash.fdir.hi = in i40e_rxd_build_fdir()
2985 txq->reg_idx = pf->fdir.fdir_vsi->base_queue; in i40e_fdir_setup_tx_resources()
2986 txq->vsi = pf->fdir.fdir_vsi; in i40e_fdir_setup_tx_resources()
2996 pf->fdir.txq = txq; in i40e_fdir_setup_tx_resources()
2997 pf->fdir.txq_available_buf_count = I40E_FDIR_PRG_PKT_CNT; in i40e_fdir_setup_tx_resources()
3043 rxq->reg_idx = pf->fdir.fdir_vsi->base_queue; in i40e_fdir_setup_rx_resources()
3044 rxq->vsi = pf->fdir.fdir_vsi; in i40e_fdir_setup_rx_resources()
[all …]
/f-stack/dpdk/drivers/net/enic/
H A Denic_clsf.c47 enic->fdir.modes = (uint32_t)RTE_FDIR_MODE_PERFECT; in enic_fdir_info()
57 enic->fdir.copy_fltr_fn = copy_fltr_v2; in enic_fdir_info()
59 enic->fdir.copy_fltr_fn = copy_fltr_v1; in enic_fdir_info()
303 key = enic->fdir.nodes[index]; in enic_clsf_destroy()
308 enic->fdir.nodes[index] = NULL; in enic_clsf_destroy()
312 if (enic->fdir.hash) { in enic_clsf_destroy()
313 rte_hash_free(enic->fdir.hash); in enic_clsf_destroy()
314 enic->fdir.hash = NULL; in enic_clsf_destroy()
331 memset(&enic->fdir.stats, 0, sizeof(enic->fdir.stats)); in enic_clsf_init()
332 enic->fdir.stats.free = ENICPMD_FDIR_MAX; in enic_clsf_init()
[all …]
H A Denic_rxtx_common.h233 mbuf->hash.fdir.hi = filter_id - 1; in enic_cq_rx_to_pkt_flags()
/f-stack/dpdk/app/test/
H A Dprocess.h69 int fd, fdir; in process_dup() local
82 fdir = dirfd(dir); in process_dup()
83 if (fdir < 0) { in process_dup()
87 fdir, procdir, in process_dup()
100 if (fd == fdir || fd <= 2) in process_dup()
/f-stack/dpdk/drivers/net/ice/
H A Dice_fdir_filter.c464 if (pf->fdir.fdir_vsi) { in ice_fdir_setup()
475 pf->fdir.fdir_vsi = vsi; in ice_fdir_setup()
533 pf->fdir.mz = mz; in ice_fdir_setup()
549 pf->fdir.mz = NULL; in ice_fdir_setup()
552 pf->fdir.rxq = NULL; in ice_fdir_setup()
555 pf->fdir.txq = NULL; in ice_fdir_setup()
640 vsi = pf->fdir.fdir_vsi; in ice_fdir_teardown()
661 pf->fdir.txq = NULL; in ice_fdir_teardown()
663 pf->fdir.rxq = NULL; in ice_fdir_teardown()
669 if (pf->fdir.mz) { in ice_fdir_teardown()
[all …]
H A Dice_rxtx_vec_avx2.c501 rx_pkts[i + 0]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
504 rx_pkts[i + 1]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
507 rx_pkts[i + 2]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
510 rx_pkts[i + 3]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
513 rx_pkts[i + 4]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
516 rx_pkts[i + 5]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
519 rx_pkts[i + 6]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
522 rx_pkts[i + 7]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx2()
H A Dice_rxtx_vec_avx512.c484 rx_pkts[i + 0]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
487 rx_pkts[i + 1]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
490 rx_pkts[i + 2]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
493 rx_pkts[i + 3]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
496 rx_pkts[i + 4]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
499 rx_pkts[i + 5]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
502 rx_pkts[i + 6]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
505 rx_pkts[i + 7]->hash.fdir.hi = in _ice_recv_raw_pkts_vec_avx512()
H A Dice_rxtx_vec_sse.c198 rx_pkts[0]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
201 rx_pkts[1]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
204 rx_pkts[2]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
207 rx_pkts[3]->hash.fdir.hi = in ice_rx_desc_to_olflags_v()
H A Dice_rxtx.c766 rxq = pf->fdir.rxq; in ice_fdir_rx_queue_start()
809 txq = pf->fdir.txq; in ice_fdir_tx_queue_start()
969 rxq = pf->fdir.rxq; in ice_fdir_rx_queue_stop()
994 txq = pf->fdir.txq; in ice_fdir_tx_queue_stop()
2097 txq->reg_idx = pf->fdir.fdir_vsi->base_queue; in ice_fdir_setup_tx_resources()
2098 txq->vsi = pf->fdir.fdir_vsi; in ice_fdir_setup_tx_resources()
2107 pf->fdir.txq = txq; in ice_fdir_setup_tx_resources()
2156 rxq->vsi = pf->fdir.fdir_vsi; in ice_fdir_setup_rx_resources()
2168 pf->fdir.rxq = rxq; in ice_fdir_setup_rx_resources()
3965 struct ice_tx_queue *txq = pf->fdir.txq; in ice_fdir_programming()
[all …]
/f-stack/dpdk/drivers/net/hns3/
H A Dhns3_fdir.c314 switch (pf->fdir.fd_cfg.fd_mode) { in hns3_init_fd_config()
316 pf->fdir.fd_cfg.max_key_length = MAX_KEY_LENGTH; in hns3_init_fd_config()
324 pf->fdir.fd_cfg.fd_mode); in hns3_init_fd_config()
357 &pf->fdir.fd_cfg.rule_num[HNS3_FD_STAGE_1], in hns3_init_fd_config()
358 &pf->fdir.fd_cfg.rule_num[HNS3_FD_STAGE_2], in hns3_init_fd_config()
359 &pf->fdir.fd_cfg.cnt_num[HNS3_FD_STAGE_1], in hns3_init_fd_config()
813 struct hns3_fdir_info *fdir_info = &pf->fdir; in hns3_fdir_filter_init()
856 struct hns3_fdir_info *fdir_info = &pf->fdir; in hns3_fdir_filter_uninit()
959 struct hns3_fdir_info *fdir_info = &pf->fdir; in hns3_fdir_filter_program()
1026 struct hns3_fdir_info *fdir_info = &pf->fdir; in hns3_clear_all_fdir_filter()
[all …]
/f-stack/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()
/f-stack/dpdk/app/test-pmd/
H A Dutil.c136 mb->hash.fdir.hi); in dump_pkt_burst()
139 mb->hash.fdir.hi, mb->hash.fdir.lo); in dump_pkt_burst()
142 mb->hash.fdir.hash, mb->hash.fdir.id); in dump_pkt_burst()
/f-stack/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_avx2.c969 rx_pkts[i + 0]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
972 rx_pkts[i + 1]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
975 rx_pkts[i + 2]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
978 rx_pkts[i + 3]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
981 rx_pkts[i + 4]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
984 rx_pkts[i + 5]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
987 rx_pkts[i + 6]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
990 rx_pkts[i + 7]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx2_flex_rxd()
H A Diavf_rxtx_vec_avx512.c979 rx_pkts[i + 0]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
982 rx_pkts[i + 1]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
985 rx_pkts[i + 2]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
988 rx_pkts[i + 3]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
991 rx_pkts[i + 4]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
994 rx_pkts[i + 5]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
997 rx_pkts[i + 6]->hash.fdir.hi = in _iavf_recv_raw_pkts_vec_avx512_flex_rxd()
1000 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()
/f-stack/dpdk/drivers/net/bnxt/
H A Dbnxt_rxr.c165 mbuf->hash.fdir.id = rte_le_to_cpu_16(tpa_start1->cfa_code); in bnxt_tpa_start()
608 mbuf->hash.fdir.hi = mark_id; in bnxt_ulp_set_mark_in_mbuf()
610 mbuf->hash.fdir.id = rxcmp1->cfa_code; in bnxt_ulp_set_mark_in_mbuf()
616 mbuf->hash.fdir.hi = 0; in bnxt_ulp_set_mark_in_mbuf()
617 mbuf->hash.fdir.id = 0; in bnxt_ulp_set_mark_in_mbuf()
657 mbuf->hash.fdir.hi = bp->mark_table[cfa_code].mark_id; in bnxt_set_mark_in_mbuf()
/f-stack/dpdk/lib/librte_mbuf/
H A Drte_mbuf_core.h567 } fdir; /**< Filter identifier if FDIR enabled */ member
/f-stack/dpdk/drivers/net/qede/
H A Dqede_filter.c147 struct rte_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()
/f-stack/dpdk/drivers/net/ixgbe/
H A Dixgbe_ethdev.h482 struct ixgbe_hw_fdir_info fdir; member
544 (&((struct ixgbe_adapter *)adapter)->fdir)

12