Home
last modified time | relevance | path

Searched refs:rused (Results 1 – 3 of 3) sorted by relevance

/f-stack/dpdk/drivers/net/virtio/
H A Dvirtio_rxtx_simple_neon.c48 struct vring_used_elem *rused; in virtio_recv_pkts_vec() local
97 rused = &vq->vq_split.ring.used->ring[desc_idx]; in virtio_recv_pkts_vec()
101 rte_prefetch_non_temporal(rused); in virtio_recv_pkts_vec()
118 desc[0] = vld1q_u64((uint64_t *)(rused + 0)); in virtio_recv_pkts_vec()
122 desc[1] = vld1q_u64((uint64_t *)(rused + 2)); in virtio_recv_pkts_vec()
126 desc[2] = vld1q_u64((uint64_t *)(rused + 4)); in virtio_recv_pkts_vec()
130 desc[3] = vld1q_u64((uint64_t *)(rused + 6)); in virtio_recv_pkts_vec()
201 rused += RTE_VIRTIO_DESC_PER_LOOP; in virtio_recv_pkts_vec()
H A Dvirtio_rxtx_simple_sse.c48 struct vring_used_elem *rused; in virtio_recv_pkts_vec() local
97 rused = &vq->vq_split.ring.used->ring[desc_idx]; in virtio_recv_pkts_vec()
101 rte_prefetch0(rused); in virtio_recv_pkts_vec()
118 desc[0] = _mm_loadu_si128((__m128i *)(rused + 0)); in virtio_recv_pkts_vec()
122 desc[1] = _mm_loadu_si128((__m128i *)(rused + 2)); in virtio_recv_pkts_vec()
126 desc[2] = _mm_loadu_si128((__m128i *)(rused + 4)); in virtio_recv_pkts_vec()
130 desc[3] = _mm_loadu_si128((__m128i *)(rused + 6)); in virtio_recv_pkts_vec()
185 rused += RTE_VIRTIO_DESC_PER_LOOP; in virtio_recv_pkts_vec()
H A Dvirtio_rxtx_simple_altivec.c48 struct vring_used_elem *rused; in virtio_recv_pkts_vec() local
99 rused = &vq->vq_split.ring.used->ring[desc_idx]; in virtio_recv_pkts_vec()
103 rte_prefetch0(rused); in virtio_recv_pkts_vec()
120 desc[0] = vec_vsx_ld(0, (unsigned char const *)(rused + 0)); in virtio_recv_pkts_vec()
124 desc[1] = vec_vsx_ld(0, (unsigned char const *)(rused + 2)); in virtio_recv_pkts_vec()
128 desc[2] = vec_vsx_ld(0, (unsigned char const *)(rused + 4)); in virtio_recv_pkts_vec()
132 desc[3] = vec_vsx_ld(0, (unsigned char const *)(rused + 6)); in virtio_recv_pkts_vec()
195 rused += RTE_VIRTIO_DESC_PER_LOOP; in virtio_recv_pkts_vec()