Home
last modified time | relevance | path

Searched refs:mbp (Results 1 – 12 of 12) sorted by relevance

/dpdk/drivers/net/virtio/
H A Dvirtio_rxtx_simple_sse.c114 __m128i mbp[RTE_VIRTIO_DESC_PER_LOOP / 2]; in virtio_recv_pkts_vec() local
117 mbp[0] = _mm_loadu_si128((__m128i *)(sw_ring + 0)); in virtio_recv_pkts_vec()
119 _mm_storeu_si128((__m128i *)&rx_pkts[0], mbp[0]); in virtio_recv_pkts_vec()
121 mbp[1] = _mm_loadu_si128((__m128i *)(sw_ring + 2)); in virtio_recv_pkts_vec()
123 _mm_storeu_si128((__m128i *)&rx_pkts[2], mbp[1]); in virtio_recv_pkts_vec()
125 mbp[2] = _mm_loadu_si128((__m128i *)(sw_ring + 4)); in virtio_recv_pkts_vec()
127 _mm_storeu_si128((__m128i *)&rx_pkts[4], mbp[2]); in virtio_recv_pkts_vec()
129 mbp[3] = _mm_loadu_si128((__m128i *)(sw_ring + 6)); in virtio_recv_pkts_vec()
131 _mm_storeu_si128((__m128i *)&rx_pkts[6], mbp[3]); in virtio_recv_pkts_vec()
H A Dvirtio_rxtx_simple_altivec.c116 __vector unsigned char mbp[RTE_VIRTIO_DESC_PER_LOOP / 2]; in virtio_recv_pkts_vec() local
119 mbp[0] = vec_vsx_ld(0, (unsigned char const *)(sw_ring + 0)); in virtio_recv_pkts_vec()
121 *(__vector unsigned char *)&rx_pkts[0] = mbp[0]; in virtio_recv_pkts_vec()
123 mbp[1] = vec_vsx_ld(0, (unsigned char const *)(sw_ring + 2)); in virtio_recv_pkts_vec()
125 *(__vector unsigned char *)&rx_pkts[2] = mbp[1]; in virtio_recv_pkts_vec()
127 mbp[2] = vec_vsx_ld(0, (unsigned char const *)(sw_ring + 4)); in virtio_recv_pkts_vec()
129 *(__vector unsigned char *)&rx_pkts[4] = mbp[2]; in virtio_recv_pkts_vec()
131 mbp[3] = vec_vsx_ld(0, (unsigned char const *)(sw_ring + 6)); in virtio_recv_pkts_vec()
133 *(__vector unsigned char *)&rx_pkts[6] = mbp[3]; in virtio_recv_pkts_vec()
H A Dvirtio_rxtx_simple_neon.c114 uint64x2_t mbp[RTE_VIRTIO_DESC_PER_LOOP / 2]; in virtio_recv_pkts_vec() local
117 mbp[0] = vld1q_u64((uint64_t *)(sw_ring + 0)); in virtio_recv_pkts_vec()
119 vst1q_u64((uint64_t *)&rx_pkts[0], mbp[0]); in virtio_recv_pkts_vec()
121 mbp[1] = vld1q_u64((uint64_t *)(sw_ring + 2)); in virtio_recv_pkts_vec()
123 vst1q_u64((uint64_t *)&rx_pkts[2], mbp[1]); in virtio_recv_pkts_vec()
125 mbp[2] = vld1q_u64((uint64_t *)(sw_ring + 4)); in virtio_recv_pkts_vec()
127 vst1q_u64((uint64_t *)&rx_pkts[4], mbp[2]); in virtio_recv_pkts_vec()
129 mbp[3] = vld1q_u64((uint64_t *)(sw_ring + 6)); in virtio_recv_pkts_vec()
131 vst1q_u64((uint64_t *)&rx_pkts[6], mbp[3]); in virtio_recv_pkts_vec()
H A Dvirtio_rxtx_packed_neon.h208 uint64x2x2_t mbp[PACKED_BATCH_SIZE / 2]; in virtqueue_dequeue_batch_packed_vec() local
235 mbp[0] = vld2q_u64((uint64_t *)&vq->vq_descx[id]); in virtqueue_dequeue_batch_packed_vec()
236 vst1q_u64((uint64_t *)&rx_pkts[0], mbp[0].val[0]); in virtqueue_dequeue_batch_packed_vec()
238 mbp[1] = vld2q_u64((uint64_t *)&vq->vq_descx[id + 2]); in virtqueue_dequeue_batch_packed_vec()
239 vst1q_u64((uint64_t *)&rx_pkts[2], mbp[1].val[0]); in virtqueue_dequeue_batch_packed_vec()
/dpdk/app/test-pmd/
H A Dtxonly.c190 pkt_burst_prepare(struct rte_mbuf *pkt, struct rte_mempool *mbp, in pkt_burst_prepare() argument
206 if (rte_mempool_get_bulk(mbp, (void **)pkt_segs, nb_segs - 1)) in pkt_burst_prepare()
333 struct rte_mempool *mbp; in pkt_burst_transmit() local
345 mbp = current_fwd_lcore()->mbp; in pkt_burst_transmit()
364 if (rte_mempool_get_bulk(mbp, (void **)pkts_burst, in pkt_burst_transmit()
367 if (unlikely(!pkt_burst_prepare(pkts_burst[nb_pkt], mbp, in pkt_burst_transmit()
372 rte_mempool_put_bulk(mbp, in pkt_burst_transmit()
380 pkt = rte_mbuf_raw_alloc(mbp); in pkt_burst_transmit()
383 if (unlikely(!pkt_burst_prepare(pkt, mbp, &eth_hdr, in pkt_burst_transmit()
H A Dflowgen.c67 struct rte_mempool *mbp; in pkt_burst_flow_gen() local
96 mbp = current_fwd_lcore()->mbp; in pkt_burst_flow_gen()
115 pkt = rte_mbuf_raw_alloc(mbp); in pkt_burst_flow_gen()
H A Dtestpmd.c1622 struct rte_mempool *mbp; in init_config() local
1721 mbp = mbuf_pool_find( in init_config()
1724 if (mbp == NULL) in init_config()
1725 mbp = mbuf_pool_find(0, 0); in init_config()
1726 fwd_lcores[lc_id]->mbp = mbp; in init_config()
1729 fwd_lcores[lc_id]->gso_ctx.direct_pool = mbp; in init_config()
1730 fwd_lcores[lc_id]->gso_ctx.indirect_pool = mbp; in init_config()
H A Dcsumonly.c713 mp = current_fwd_lcore()->mbp; in pkt_copy_split()
H A Dtestpmd.h299 struct rte_mempool *mbp; /**< The mbuf pool to use by this core */ member
/dpdk/drivers/net/mlx5/
H A Dmlx5_rxtx_vec_neon.h46 uint64x2_t mbp; in rxq_copy_mbuf_v() local
48 mbp = vld1q_u64((void *)&elts[pos]); in rxq_copy_mbuf_v()
49 vst1q_u64((void *)&pkts[pos], mbp); in rxq_copy_mbuf_v()
H A Dmlx5_rxtx_vec_sse.h48 __m128i mbp; in rxq_copy_mbuf_v() local
50 mbp = _mm_loadu_si128((__m128i *)&elts[pos]); in rxq_copy_mbuf_v()
51 _mm_storeu_si128((__m128i *)&pkts[pos], mbp); in rxq_copy_mbuf_v()
H A Dmlx5_rxtx_vec_altivec.h50 __vector unsigned char mbp; in rxq_copy_mbuf_v() local
52 mbp = (__vector unsigned char)vec_vsx_ld(0, in rxq_copy_mbuf_v()
54 *(__vector unsigned char *)&pkts[pos] = mbp; in rxq_copy_mbuf_v()