Home
last modified time | relevance | path

Searched refs:mi (Results 1 – 9 of 9) sorted by relevance

/dpdk/drivers/net/ice/base/
H A Dice_metainit.c86 mi->idx = idx; in _metainit_parse_item()
89 mi->tsr = (u8)(d64 & 0xff); in _metainit_parse_item()
90 mi->ho = (u16)((d64 >> 8) & 0x1ff); in _metainit_parse_item()
91 mi->pc = (u16)((d64 >> 17) & 0xff); in _metainit_parse_item()
92 mi->pg_rn = (u16)((d64 >> 25) & 0x3ff); in _metainit_parse_item()
93 mi->cd = (u16)((d64 >> 36) & 0x7); in _metainit_parse_item()
101 mi->gpr_b_ctrl = (d64 & 0x1) != 0; in _metainit_parse_item()
119 mi->gpr_d_id = (u8)(d64 & 0xf); in _metainit_parse_item()
122 mi->flags = d64; in _metainit_parse_item()
125 mi->flags |= (d64 << 61); in _metainit_parse_item()
[all …]
H A Dice_parser_rt.c80 struct ice_metainit_item *mi = &psr->mi_table[0]; in ice_parser_rt_reset() local
85 _rt_tsr_set(rt, mi->tsr); in ice_parser_rt_reset()
86 _rt_ho_set(rt, mi->ho); in ice_parser_rt_reset()
87 _rt_np_set(rt, mi->pc); in ice_parser_rt_reset()
88 _rt_nn_set(rt, mi->pg_rn); in ice_parser_rt_reset()
93 if ((mi->flags & (1ul << i)) != 0ul) in ice_parser_rt_reset()
/dpdk/lib/mbuf/
H A Drte_mbuf.h181 return (struct rte_mbuf *)RTE_PTR_SUB(mi->buf_addr, sizeof(*mi) + mi->priv_size); in rte_mbuf_from_indirect()
1133 mi->ol_flags = m->ol_flags; in rte_pktmbuf_attach()
1134 mi->shinfo = m->shinfo; in rte_pktmbuf_attach()
1144 mi->data_off = m->data_off; in rte_pktmbuf_attach()
1145 mi->data_len = m->data_len; in rte_pktmbuf_attach()
1146 mi->buf_iova = m->buf_iova; in rte_pktmbuf_attach()
1147 mi->buf_addr = m->buf_addr; in rte_pktmbuf_attach()
1148 mi->buf_len = m->buf_len; in rte_pktmbuf_attach()
1150 mi->next = NULL; in rte_pktmbuf_attach()
1151 mi->pkt_len = mi->data_len; in rte_pktmbuf_attach()
[all …]
H A Drte_mbuf.c514 struct rte_mbuf *mc, *mi, **prev; in rte_pktmbuf_clone() local
522 mi = mc; in rte_pktmbuf_clone()
523 prev = &mi->next; in rte_pktmbuf_clone()
529 rte_pktmbuf_attach(mi, md); in rte_pktmbuf_clone()
530 *prev = mi; in rte_pktmbuf_clone()
531 prev = &mi->next; in rte_pktmbuf_clone()
533 (mi = rte_pktmbuf_alloc(mp)) != NULL); in rte_pktmbuf_clone()
540 if (unlikely(mi == NULL)) { in rte_pktmbuf_clone()
/dpdk/lib/acl/
H A Dacl_run_avx512x16.h251 uint32_t i, k, mi; in resolve_mcgt8_avx512x1() local
262 mi = match[k] << ACL_MATCH_LOG; in resolve_mcgt8_avx512x1()
264 cr = _mm512_maskz_loadu_epi32(cm, res + mi); in resolve_mcgt8_avx512x1()
265 cp = _mm512_maskz_loadu_epi32(cm, pri + mi); in resolve_mcgt8_avx512x1()
270 mi = pm[k] << ACL_MATCH_LOG; in resolve_mcgt8_avx512x1()
272 nr = _mm512_maskz_loadu_epi32(cm, res + mi); in resolve_mcgt8_avx512x1()
273 np = _mm512_maskz_loadu_epi32(cm, pri + mi); in resolve_mcgt8_avx512x1()
H A Dacl_run_avx512.c76 uint32_t i, j, k, mi, mn; in resolve_mcle8_avx512x1() local
85 mi = match[k] << ACL_MATCH_LOG; in resolve_mcle8_avx512x1()
89 cr = _mm_loadu_si128((const xmm_t *)(res + mi + j)); in resolve_mcle8_avx512x1()
90 cp = _mm_loadu_si128((const xmm_t *)(pri + mi + j)); in resolve_mcle8_avx512x1()
H A Dacl_run_avx512_common.h393 _F_(resolve_match_idx)(_T_simd mi) in _F_()
397 return _M_I_(slli_epi32)(mi, ACL_MATCH_LOG); in _F_()
/dpdk/drivers/net/dpaa/
H A Ddpaa_rxtx.c800 struct rte_mbuf *temp, *mi; in dpaa_eth_mbuf_to_sg_fd() local
869 mi = rte_mbuf_from_indirect(cur_seg); in dpaa_eth_mbuf_to_sg_fd()
870 if (rte_mbuf_refcnt_read(mi) > 1) { in dpaa_eth_mbuf_to_sg_fd()
877 rte_mbuf_refcnt_update(mi, 1); in dpaa_eth_mbuf_to_sg_fd()
900 struct rte_mbuf *mi = NULL; in tx_on_dpaa_pool_unsegmented() local
921 mi = rte_mbuf_from_indirect(mbuf); in tx_on_dpaa_pool_unsegmented()
922 if (rte_mbuf_refcnt_read(mi) > 1) { in tx_on_dpaa_pool_unsegmented()
936 rte_mbuf_refcnt_update(mi, 1); in tx_on_dpaa_pool_unsegmented()
1056 struct rte_mbuf *mbuf, *mi = NULL; in dpaa_eth_queue_tx() local
1118 mi = rte_mbuf_from_indirect(mbuf); in dpaa_eth_queue_tx()
[all …]
/dpdk/drivers/net/dpaa2/
H A Ddpaa2_rxtx.c503 mempool_to_bpid(mi->pool)); in eth_mbuf_to_sg_fd()
504 rte_mbuf_refcnt_update(mi, 1); in eth_mbuf_to_sg_fd()
545 struct rte_mbuf *mi; in eth_mbuf_to_fd() local
548 if (rte_mbuf_refcnt_read(mi) > 1) in eth_mbuf_to_fd()
551 rte_mbuf_refcnt_update(mi, 1); in eth_mbuf_to_fd()
1218 struct rte_mbuf *mi; in dpaa2_dev_tx() local
1319 mp = mi->pool; in dpaa2_dev_tx()
1534 struct rte_mbuf *mi; in dpaa2_dev_tx_multi_txq_ordered() local
1599 mp = mi->pool; in dpaa2_dev_tx_multi_txq_ordered()
1672 struct rte_mbuf *mi; in dpaa2_dev_tx_ordered() local
[all …]