Home
last modified time | relevance | path

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

/dpdk/drivers/net/ngbe/
H A Dngbe_rxtx.h43 } qw1; /* also as r.hdr_addr */ member
85 #define NGBE_RXD_STATUS(rxd) ((rxd)->qw1.lo.status)
122 #define NGBE_RXD_LENGTH(rxd) ((rxd)->qw1.hi.len)
123 #define NGBE_RXD_VLAN(rxd) ((rxd)->qw1.hi.tag)
H A Dngbe_rxtx.c1010 status = rxdp->qw1.lo.status; in ngbe_rx_scan_hw_ring()
1023 s[j] = rte_le_to_cpu_32(rxdp[j].qw1.lo.status); in ngbe_rx_scan_hw_ring()
1040 pkt_len = rte_le_to_cpu_16(rxdp[j].qw1.hi.len) - in ngbe_rx_scan_hw_ring()
1270 staterr = rxdp->qw1.lo.status; in ngbe_recv_pkts()
1305 (uint16_t)rte_le_to_cpu_16(rxd.qw1.hi.len)); in ngbe_recv_pkts()
1367 rxm->vlan_tci = rte_le_to_cpu_16(rxd.qw1.hi.tag); in ngbe_recv_pkts()
1494 staterr = rte_le_to_cpu_32(rxdp->qw1.lo.status); in ngbe_recv_pkts_sc()
1504 rte_le_to_cpu_16(rxd.qw1.hi.len)); in ngbe_recv_pkts_sc()
1576 data_len = rte_le_to_cpu_16(rxd.qw1.hi.len); in ngbe_recv_pkts_sc()
2388 (rxdp->qw1.lo.status & in ngbe_dev_rx_queue_count()
[all …]
/dpdk/drivers/net/txgbe/
H A Dtxgbe_rxtx.h43 } qw1; /* also as r.hdr_addr */ member
89 #define TXGBE_RXD_STATUS(rxd) ((rxd)->qw1.lo.status)
145 #define TXGBE_RXD_LENGTH(rxd) ((rxd)->qw1.hi.len)
146 #define TXGBE_RXD_VLAN(rxd) ((rxd)->qw1.hi.tag)
H A Dtxgbe_rxtx.c1203 status = rxdp->qw1.lo.status; in txgbe_rx_scan_hw_ring()
1216 s[j] = rte_le_to_cpu_32(rxdp[j].qw1.lo.status); in txgbe_rx_scan_hw_ring()
1233 pkt_len = rte_le_to_cpu_16(rxdp[j].qw1.hi.len) - in txgbe_rx_scan_hw_ring()
1470 staterr = rxdp->qw1.lo.status; in txgbe_recv_pkts()
1505 (uint16_t)rte_le_to_cpu_16(rxd.qw1.hi.len)); in txgbe_recv_pkts()
1566 rxm->vlan_tci = rte_le_to_cpu_16(rxd.qw1.hi.tag); in txgbe_recv_pkts()
1746 staterr = rte_le_to_cpu_32(rxdp->qw1.lo.status); in txgbe_recv_pkts_lro()
1756 rte_le_to_cpu_16(rxd.qw1.hi.len)); in txgbe_recv_pkts_lro()
1828 data_len = rte_le_to_cpu_16(rxd.qw1.hi.len); in txgbe_recv_pkts_lro()
2722 (rxdp->qw1.lo.status & in txgbe_dev_rx_queue_count()
[all …]
/dpdk/lib/net/
H A Dnet_crc_avx512.c181 __m512i qw0 = _mm512_set1_epi64(0), qw1, qw2, qw3; in crc32_eth_calc_vpclmulqdq() local
202 qw1 = _mm512_loadu_si512((const __m512i *) in crc32_eth_calc_vpclmulqdq()
209 fold1 = crcr32_folding_round(qw1, k, fold1); in crc32_eth_calc_vpclmulqdq()
/dpdk/drivers/net/iavf/
H A Diavf_ipsec_crypto.h18 __le64 qw1; member
H A Diavf_rxtx.c2418 __le64 qw1; member
2429 desc_qws->qw1 = IAVF_TX_DESC_DTYPE_CONTEXT; in iavf_fill_context_desc()
2432 iavf_fill_ctx_desc_cmd_field(&desc_qws->qw1, m, vlan_flag); in iavf_fill_context_desc()
2438 iavf_fill_ctx_desc_ipsec_field(&desc_qws->qw1, in iavf_fill_context_desc()
2441 *tlen = iavf_fill_ctx_desc_segmentation_field(&desc_qws->qw1, in iavf_fill_context_desc()
2452 desc_qws->qw1 = rte_cpu_to_le_64(desc_qws->qw1); in iavf_fill_context_desc()
2469 desc->qw1 = rte_cpu_to_le_64(((uint64_t)md->sa_idx << in iavf_fill_ipsec_desc()
2492 iavf_build_data_desc_cmd_offset_fields(volatile uint64_t *qw1, in iavf_build_data_desc_cmd_offset_fields() argument
2499 *qw1 = IAVF_TX_DESC_DTYPE_DATA; in iavf_build_data_desc_cmd_offset_fields()
2550 *qw1 = rte_cpu_to_le_64((((uint64_t)command << in iavf_build_data_desc_cmd_offset_fields()
/dpdk/drivers/net/ice/base/
H A Dice_lan_tx_rx.h1074 __le64 qw1; member
/dpdk/drivers/net/ice/
H A Dice_rxtx.c2855 ctx_txd->qw1 = in ice_xmit_pkts()