Home
last modified time | relevance | path

Searched refs:txbd (Results 1 – 5 of 5) sorted by relevance

/dpdk/drivers/net/bnxt/
H A Dbnxt_txr.c134 struct tx_bd_long *txbd; in bnxt_start_xmit() local
188 txbd = &txr->tx_desc_ring[prod]; in bnxt_start_xmit()
189 txbd->opaque = *coal_pkts; in bnxt_start_xmit()
191 txbd->flags_type |= TX_BD_SHORT_FLAGS_COAL_NOW; in bnxt_start_xmit()
192 txbd->flags_type |= TX_BD_LONG_FLAGS_NO_CMPL; in bnxt_start_xmit()
193 txbd->len = tx_pkt->data_len; in bnxt_start_xmit()
199 *last_txbd = txbd; in bnxt_start_xmit()
202 txbd->flags_type |= TX_BD_LONG_TYPE_TX_BD_LONG; in bnxt_start_xmit()
340 txbd = &txr->tx_desc_ring[prod]; in bnxt_start_xmit()
343 txbd->len = m_seg->data_len; in bnxt_start_xmit()
[all …]
H A Dbnxt_rxtx_vec_sse.c358 _mm_store_si128((void *)txbd, desc); in bnxt_xmit_one()
367 struct tx_bd_long *txbd; in bnxt_xmit_fixed_burst_vec() local
372 txbd = &txr->tx_desc_ring[tx_prod]; in bnxt_xmit_fixed_burst_vec()
376 rte_prefetch0(txbd); in bnxt_xmit_fixed_burst_vec()
377 rte_prefetch0(txbd + 3); in bnxt_xmit_fixed_burst_vec()
388 rte_prefetch0(txbd + 4); in bnxt_xmit_fixed_burst_vec()
389 rte_prefetch0(txbd + 7); in bnxt_xmit_fixed_burst_vec()
391 bnxt_xmit_one(tx_pkts[0], txbd++, tx_buf++); in bnxt_xmit_fixed_burst_vec()
392 bnxt_xmit_one(tx_pkts[1], txbd++, tx_buf++); in bnxt_xmit_fixed_burst_vec()
393 bnxt_xmit_one(tx_pkts[2], txbd++, tx_buf++); in bnxt_xmit_fixed_burst_vec()
[all …]
H A Dbnxt_rxtx_vec_avx2.c432 _mm_store_si128((void *)txbd, desc); in bnxt_xmit_one()
441 struct tx_bd_long *txbd; in bnxt_xmit_fixed_burst_vec() local
446 txbd = &txr->tx_desc_ring[tx_prod]; in bnxt_xmit_fixed_burst_vec()
450 rte_prefetch0(txbd); in bnxt_xmit_fixed_burst_vec()
451 rte_prefetch0(txbd + 3); in bnxt_xmit_fixed_burst_vec()
466 bnxt_xmit_one(pkts[0], txbd++, tx_buf++); in bnxt_xmit_fixed_burst_vec()
481 rte_prefetch0(txbd + 4); in bnxt_xmit_fixed_burst_vec()
482 rte_prefetch0(txbd + 7); in bnxt_xmit_fixed_burst_vec()
517 _mm256_store_si256((void *)txbd, dsc01); in bnxt_xmit_fixed_burst_vec()
522 txbd += BNXT_TX_DESCS_PER_LOOP; in bnxt_xmit_fixed_burst_vec()
[all …]
H A Dbnxt_rxtx_vec_neon.c381 struct tx_bd_long *txbd = NULL; in bnxt_xmit_fixed_burst_vec() local
400 txbd = &txr->tx_desc_ring[tx_prod]; in bnxt_xmit_fixed_burst_vec()
401 txbd->address = tx_mbuf->buf_iova + tx_mbuf->data_off; in bnxt_xmit_fixed_burst_vec()
402 txbd->len = tx_mbuf->data_len; in bnxt_xmit_fixed_burst_vec()
403 txbd->flags_type = bnxt_xmit_flags_len(tx_mbuf->data_len, in bnxt_xmit_fixed_burst_vec()
410 if (txbd) { in bnxt_xmit_fixed_burst_vec()
411 txbd->opaque = nb_pkts; in bnxt_xmit_fixed_burst_vec()
412 txbd->flags_type &= ~TX_BD_LONG_FLAGS_NO_CMPL; in bnxt_xmit_fixed_burst_vec()
/dpdk/drivers/net/enetc/
H A Denetc_rxtx.c86 struct enetc_tx_bd *txbd; in enetc_xmit_pkts() local
98 txbd = ENETC_TXBD(*tx_ring, i); in enetc_xmit_pkts()
100 txbd->frm_len = tx_pkts[start]->pkt_len; in enetc_xmit_pkts()
101 txbd->buf_len = txbd->frm_len; in enetc_xmit_pkts()
102 txbd->flags = rte_cpu_to_le_16(ENETC_TXBD_FLAGS_F); in enetc_xmit_pkts()
103 txbd->addr = (uint64_t)(uintptr_t) in enetc_xmit_pkts()