Home
last modified time | relevance | path

Searched refs:head_size (Results 1 – 4 of 4) sorted by relevance

/dpdk/drivers/net/virtio/
H A Dvirtio_rxtx_packed_neon.h24 uint16_t head_size = vq->hw->vtnet_hdr_size; in virtqueue_enqueue_batch_packed_vec() local
79 uint16x4_t head_rooms = vdup_n_u16(head_size); in virtqueue_enqueue_batch_packed_vec()
94 tx_pkts[i]->data_off -= head_size; in virtqueue_enqueue_batch_packed_vec()
95 tx_pkts[i]->data_len += head_size; in virtqueue_enqueue_batch_packed_vec()
128 struct virtio_net_hdr *, -head_size); in virtqueue_enqueue_batch_packed_vec()
136 struct virtio_net_hdr *, -head_size); in virtqueue_enqueue_batch_packed_vec()
168 uint16_t head_size = hw->vtnet_hdr_size; in virtqueue_dequeue_batch_packed_vec() local
201 head_size, /* sub head_size on pkt_len */ in virtqueue_dequeue_batch_packed_vec()
203 head_size, /* sub head_size on data_len */ in virtqueue_dequeue_batch_packed_vec()
274 RTE_PKTMBUF_HEADROOM - head_size; in virtqueue_dequeue_batch_packed_vec()
H A Dvirtio_rxtx_packed_avx.h24 uint16_t head_size = vq->hw->vtnet_hdr_size; in virtqueue_enqueue_batch_packed_vec() local
46 __m256i head_rooms = _mm256_set1_epi16(head_size); in virtqueue_enqueue_batch_packed_vec()
69 tx_pkts[i]->data_off -= head_size; in virtqueue_enqueue_batch_packed_vec()
70 tx_pkts[i]->data_len += head_size; in virtqueue_enqueue_batch_packed_vec()
105 struct virtio_net_hdr *, -head_size); in virtqueue_enqueue_batch_packed_vec()
117 struct virtio_net_hdr *, -head_size); in virtqueue_enqueue_batch_packed_vec()
H A Dvirtio_rxtx.c451 int16_t head_size = vq->hw->vtnet_hdr_size; in virtqueue_enqueue_xmit_inorder() local
465 struct virtio_net_hdr *, -head_size); in virtqueue_enqueue_xmit_inorder()
474 start_dp[idx].len = cookies[i]->data_len + head_size; in virtqueue_enqueue_xmit_inorder()
497 int16_t head_size = vq->hw->vtnet_hdr_size; in virtqueue_enqueue_xmit_packed_fast() local
512 -head_size); in virtqueue_enqueue_xmit_packed_fast()
520 dp->addr = VIRTIO_MBUF_DATA_DMA_ADDR(cookie, vq) - head_size; in virtqueue_enqueue_xmit_packed_fast()
521 dp->len = cookie->data_len + head_size; in virtqueue_enqueue_xmit_packed_fast()
551 int16_t head_size = vq->hw->vtnet_hdr_size; in virtqueue_enqueue_xmit() local
569 -head_size); in virtqueue_enqueue_xmit()
611 start_dp[idx].addr -= head_size; in virtqueue_enqueue_xmit()
[all …]
H A Dvirtqueue.h719 int16_t head_size = vq->hw->vtnet_hdr_size; in virtqueue_enqueue_xmit_packed() local
743 -head_size); in virtqueue_enqueue_xmit_packed()
796 start_dp[idx].addr -= head_size; in virtqueue_enqueue_xmit_packed()
797 start_dp[idx].len += head_size; in virtqueue_enqueue_xmit_packed()