Home
last modified time | relevance | path

Searched refs:qw0 (Results 1 – 7 of 7) sorted by relevance

/dpdk/drivers/net/txgbe/
H A Dtxgbe_rxtx.h28 } qw0; /* also as r.pkt_addr */ member
79 #define TXGBE_RXD_RSSHASH(rxd) ((rxd)->qw0.dw1)
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)
205 __le64 qw0; /* r.buffer_addr , w.reserved */ member
H A Dtxgbe_rxtx.c164 txdp->qw0 = rte_cpu_to_le_64(buf_dma_addr); in tx4()
184 txdp->qw0 = cpu_to_le64(buf_dma_addr); in tx1()
995 txd->qw0 = rte_cpu_to_le_64(buf_dma_addr); in txgbe_xmit_pkts()
1252 rte_le_to_cpu_32(rxdp[j].qw0.dw1); in txgbe_rx_scan_hw_ring()
1255 rte_le_to_cpu_16(rxdp[j].qw0.hi.csum) & in txgbe_rx_scan_hw_ring()
1258 rte_le_to_cpu_16(rxdp[j].qw0.hi.ipid); in txgbe_rx_scan_hw_ring()
1564 pkt_info = rte_le_to_cpu_32(rxd.qw0.dw0); in txgbe_recv_pkts()
1577 rxm->hash.rss = rte_le_to_cpu_32(rxd.qw0.dw1); in txgbe_recv_pkts()
1580 rte_le_to_cpu_16(rxd.qw0.hi.csum) & in txgbe_recv_pkts()
1644 pkt_info = rte_le_to_cpu_32(desc->qw0.dw0); in txgbe_fill_cluster_head_buf()
[all …]
/dpdk/drivers/net/ngbe/
H A Dngbe_rxtx.h28 } qw0; /* also as r.pkt_addr */ member
78 #define NGBE_RXD_RSSHASH(rxd) ((rxd)->qw0.dw1)
81 #define NGBE_RXD_IPID(rxd) ((rxd)->qw0.hi.ipid)
82 #define NGBE_RXD_CSUM(rxd) ((rxd)->qw0.hi.csum)
172 rte_le64_t qw0; /* r.buffer_addr , w.reserved */ member
H A Dngbe_rxtx.c121 txdp->qw0 = rte_cpu_to_le_64(buf_dma_addr); in tx4()
141 txdp->qw0 = cpu_to_le64(buf_dma_addr); in tx1()
814 txd->qw0 = rte_cpu_to_le_64(buf_dma_addr); in ngbe_xmit_pkts()
1033 pkt_info[j] = rte_le_to_cpu_32(rxdp[j].qw0.dw0); in ngbe_rx_scan_hw_ring()
1059 rte_le_to_cpu_32(rxdp[j].qw0.dw1); in ngbe_rx_scan_hw_ring()
1365 pkt_info = rte_le_to_cpu_32(rxd.qw0.dw0); in ngbe_recv_pkts()
1378 rxm->hash.rss = rte_le_to_cpu_32(rxd.qw0.dw1); in ngbe_recv_pkts()
1440 pkt_info = rte_le_to_cpu_32(desc->qw0.dw0); in ngbe_fill_cluster_head_buf()
1449 head->hash.rss = rte_le_to_cpu_32(desc->qw0.dw1); in ngbe_fill_cluster_head_buf()
/dpdk/lib/net/
H A Dnet_crc_avx512.c181 __m512i qw0 = _mm512_set1_epi64(0), qw1, qw2, qw3; in crc32_eth_calc_vpclmulqdq() local
201 qw0 = _mm512_loadu_si512((const __m512i *)&data[n]); in crc32_eth_calc_vpclmulqdq()
208 fold0 = crcr32_folding_round(qw0, k, fold0); in crc32_eth_calc_vpclmulqdq()
/dpdk/drivers/net/iavf/
H A Diavf_ipsec_crypto.h17 __le64 qw0; member
H A Diavf_rxtx.c2350 iavf_fill_ctx_desc_tunnelling_field(volatile uint64_t *qw0, in iavf_fill_ctx_desc_tunnelling_field() argument
2375 *qw0 = eip_typ << IAVF_TXD_CTX_QW0_TUN_PARAMS_EIPT_SHIFT | in iavf_fill_ctx_desc_tunnelling_field()
2417 __le64 qw0; member
2447 iavf_fill_ctx_desc_tunnelling_field(&desc_qws->qw0, m); in iavf_fill_context_desc()
2449 desc_qws->qw0 = 0; in iavf_fill_context_desc()
2451 desc_qws->qw0 = rte_cpu_to_le_64(desc_qws->qw0); in iavf_fill_context_desc()
2463 desc->qw0 = rte_cpu_to_le_64(((uint64_t)md->l4_payload_len << in iavf_fill_ipsec_desc()