Searched refs:descs (Results 1 - 14 of 14) sorted by relevance

/deb_dpdk/drivers/net/i40e/
H A Di40e_rxtx_vec_sse.c140 desc_to_olflags_v(__m128i descs[4], struct rte_mbuf **rx_pkts) argument
189 vlan0 = _mm_unpackhi_epi32(descs[0], descs[1]);
190 vlan1 = _mm_unpackhi_epi32(descs[2], descs[3]);
221 desc_to_ptype_v(__m128i descs[4], struct rte_mbuf **rx_pkts) argument
223 __m128i ptype0 = _mm_unpackhi_epi64(descs[0], descs[1]);
224 __m128i ptype1 = _mm_unpackhi_epi64(descs[2], descs[
320 __m128i descs[RTE_I40E_DESCS_PER_LOOP]; local
[all...]
H A Di40e_rxtx_vec_altivec.c142 desc_to_olflags_v(vector unsigned long descs[4], struct rte_mbuf **rx_pkts) argument
179 vlan0 = (vector unsigned int)vec_mergel(descs[0], descs[1]);
180 vlan1 = (vector unsigned int)vec_mergel(descs[2], descs[3]);
212 desc_to_ptype_v(vector unsigned long descs[4], struct rte_mbuf **rx_pkts) argument
214 vector unsigned long ptype0 = vec_mergel(descs[0], descs[1]);
215 vector unsigned long ptype1 = vec_mergel(descs[2], descs[
316 vector unsigned long descs[RTE_I40E_DESCS_PER_LOOP]; local
[all...]
H A Di40e_rxtx_vec_neon.c128 desc_to_olflags_v(uint64x2_t descs[4], struct rte_mbuf **rx_pkts) argument
163 vlan0 = vzipq_u32(vreinterpretq_u32_u64(descs[0]),
164 vreinterpretq_u32_u64(descs[2])).val[1];
165 vlan1 = vzipq_u32(vreinterpretq_u32_u64(descs[1]),
166 vreinterpretq_u32_u64(descs[3])).val[1];
191 #define desc_to_olflags_v(descs, rx_pkts) do {} while (0)
198 desc_to_ptype_v(uint64x2_t descs[4], struct rte_mbuf **rx_pkts) argument
205 tmp = vreinterpretq_u8_u64(vshrq_n_u64(descs[i], 30));
295 uint64x2_t descs[RTE_I40E_DESCS_PER_LOOP]; local
309 descs[
[all...]
/deb_dpdk/drivers/net/ixgbe/
H A Dixgbe_rxtx_vec_sse.c145 desc_to_olflags_v(__m128i descs[4], uint8_t vlan_flags, argument
199 ptype0 = _mm_unpacklo_epi16(descs[0], descs[1]);
200 ptype1 = _mm_unpacklo_epi16(descs[2], descs[3]);
201 vtag0 = _mm_unpackhi_epi16(descs[0], descs[1]);
202 vtag1 = _mm_unpackhi_epi16(descs[2], descs[3]);
335 __m128i descs[RTE_IXGBE_DESCS_PER_LOO local
[all...]
H A Dixgbe_rxtx_vec_neon.c251 uint64x2_t descs[RTE_IXGBE_DESCS_PER_LOOP]; local
269 /* A. load 4 pkts descs */
270 descs[0] = vld1q_u64((uint64_t *)(rxdp));
271 descs[1] = vld1q_u64((uint64_t *)(rxdp + 1));
272 descs[2] = vld1q_u64((uint64_t *)(rxdp + 2));
273 descs[3] = vld1q_u64((uint64_t *)(rxdp + 3));
287 pkt_mb4 = vqtbl1q_u8(vreinterpretq_u8_u64(descs[3]), shuf_msk);
288 pkt_mb3 = vqtbl1q_u8(vreinterpretq_u8_u64(descs[2]), shuf_msk);
291 pkt_mb2 = vqtbl1q_u8(vreinterpretq_u8_u64(descs[1]), shuf_msk);
292 pkt_mb1 = vqtbl1q_u8(vreinterpretq_u8_u64(descs[
[all...]
/deb_dpdk/drivers/net/fm10k/
H A Dfm10k_rxtx_vec.c74 fm10k_desc_to_olflags_v(__m128i descs[4], struct rte_mbuf **rx_pkts) argument
122 ptype0 = _mm_unpacklo_epi16(descs[0], descs[1]);
123 ptype1 = _mm_unpacklo_epi16(descs[2], descs[3]);
124 vtag0 = _mm_unpackhi_epi16(descs[0], descs[1]);
125 vtag1 = _mm_unpackhi_epi16(descs[2], descs[3]);
169 fm10k_desc_to_pktype_v(__m128i descs[ argument
[all...]
/deb_dpdk/lib/librte_vhost/
H A Dvirtio_net.c343 struct vring_desc *descs, struct rte_mbuf *m,
356 desc = &descs[desc_idx];
437 desc = &descs[desc->next];
491 struct vring_desc *descs; local
542 descs = (struct vring_desc *)(uintptr_t)gpa_to_vva(dev,
544 if (unlikely(!descs)) {
559 descs = idesc;
563 sz = vq->desc[desc_idx].len / sizeof(*descs);
565 descs = vq->desc;
569 err = copy_mbuf_to_desc(dev, vq, descs, pkt
342 copy_mbuf_to_desc(struct virtio_net *dev, struct vhost_virtqueue *vq, struct vring_desc *descs, struct rte_mbuf *m, uint16_t desc_idx, uint32_t size) argument
619 struct vring_desc *descs = vq->desc; local
1114 copy_desc_to_mbuf(struct virtio_net *dev, struct vring_desc *descs, uint16_t max_desc, struct rte_mbuf *m, uint16_t desc_idx, struct rte_mempool *mbuf_pool) argument
[all...]
/deb_dpdk/drivers/net/enic/
H A Denic_rxtx.c258 cqd_ptr = (struct cq_desc *)(cq->ring.descs) + cq_idx;
281 rqd_ptr = ((struct rq_enet_desc *)rq->ring.descs) + rq_idx;
305 cqd_ptr = (struct cq_desc *)(cq->ring.descs) + cq_idx;
467 struct wq_enet_desc *descs, *desc_p, desc_tmp; local
506 descs = (struct wq_enet_desc *)wq->ring.descs;
507 desc_p = descs + head_idx;
545 desc_p = descs + head_idx;
H A Denic_main.c304 struct rq_enet_desc *rqd = rq->ring.descs;
685 "Number of rx descs too low, adjusting to minimum\n");
800 "TX Queues - effective number of descs:%d\n",
/deb_dpdk/drivers/net/ena/base/
H A Dena_eth_com.h77 u16 descs; member in struct:ena_com_rx_ctx
H A Dena_eth_com.c159 ena_trc_dbg("ena q_id: %d packets were completed. first desc idx %u descs# %d\n",
418 ena_rx_ctx->descs = nb_hw_desc;
448 ena_rx_ctx->descs = nb_hw_desc;
/deb_dpdk/drivers/net/enic/base/
H A Dvnic_dev.c266 memset(ring->descs, 0, ring->size);
301 ring->descs = (u8 *)ring->descs_unaligned +
314 if (ring->descs) {
319 ring->descs = NULL;
H A Dvnic_dev.h78 void *descs; member in struct:vnic_dev_ring
/deb_dpdk/drivers/net/ena/
H A Dena_ethdev.c1519 ena_rx_ctx.descs = 0;
1529 if (unlikely(ena_rx_ctx.descs == 0))
1532 while (segments < ena_rx_ctx.descs) {
1539 mbuf->nb_segs = ena_rx_ctx.descs;
1680 /* Get Tx info & store how many descs were processed */
1693 /* If too many descs to clean, leave it for another run */

Completed in 17 milliseconds