Home
last modified time | relevance | path

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

/dpdk/drivers/net/failsafe/
H A Dfailsafe_intr.c68 events = priv->rxp.evec; in fs_rx_event_proxy_routine()
96 rte_service_map_lcore_set(priv->rxp.sid, priv->rxp.scid, 0); in fs_rx_event_proxy_service_uninstall()
191 priv->rxp.scid, 1); in fs_rx_event_proxy_service_install()
228 priv->rxp.evec = calloc(NUM_RX_PROXIES, sizeof(*priv->rxp.evec)); in fs_rx_event_proxy_install()
241 close(priv->rxp.efd); in fs_rx_event_proxy_install()
242 priv->rxp.efd = -1; in fs_rx_event_proxy_install()
245 free(priv->rxp.evec); in fs_rx_event_proxy_install()
246 priv->rxp.evec = NULL; in fs_rx_event_proxy_install()
393 free(priv->rxp.evec); in fs_rx_event_proxy_uninstall()
397 close(priv->rxp.efd); in fs_rx_event_proxy_uninstall()
[all …]
H A Dfailsafe.c185 priv->rxp = FS_RX_PROXY_INIT; in fs_eth_dev_create()
H A Dfailsafe_private.h188 struct rx_proxy rxp; member
H A Dfailsafe_ops.c490 if (PRIV(dev)->rxp.sstate != SS_RUNNING) { in fs_rx_intr_enable()
/dpdk/drivers/net/iavf/
H A Diavf_rxtx_vec_common.h421 mb0 = rxp[0]; in iavf_rxq_rearm_common()
422 mb1 = rxp[1]; in iavf_rxq_rearm_common()
458 mb0 = rxp[0]; in iavf_rxq_rearm_common()
459 mb1 = rxp[1]; in iavf_rxq_rearm_common()
460 mb2 = rxp[2]; in iavf_rxq_rearm_common()
461 mb3 = rxp[3]; in iavf_rxq_rearm_common()
462 mb4 = rxp[4]; in iavf_rxq_rearm_common()
463 mb5 = rxp[5]; in iavf_rxq_rearm_common()
464 mb6 = rxp[6]; in iavf_rxq_rearm_common()
465 mb7 = rxp[7]; in iavf_rxq_rearm_common()
[all …]
H A Diavf_rxtx_vec_sse.c26 struct rte_mbuf **rxp = &rxq->sw_ring[rxq->rxrearm_start]; in iavf_rxq_rearm() local
35 if (rte_mempool_get_bulk(rxq->mp, (void *)rxp, in iavf_rxq_rearm()
40 rxp[i] = &rxq->fake_mbuf; in iavf_rxq_rearm()
51 for (i = 0; i < rxq->rx_free_thresh; i += 2, rxp += 2) { in iavf_rxq_rearm()
54 mb0 = rxp[0]; in iavf_rxq_rearm()
55 mb1 = rxp[1]; in iavf_rxq_rearm()
H A Diavf_rxtx_vec_avx512.c40 struct rte_mbuf **rxp = &rxq->sw_ring[rxq->rxrearm_start]; in iavf_rxq_rearm() local
70 rxp[i] = &rxq->fake_mbuf; in iavf_rxq_rearm()
100 _mm512_storeu_si512(rxp, mbuf_ptrs); in iavf_rxq_rearm()
144 rxp += IAVF_DESCS_PER_LOOP_AVX; in iavf_rxq_rearm()
/dpdk/app/test-pmd/
H A Dconfig.c4013 return rxp; in fwd_topology_tx_port_get()
4015 return rxp - 1; in fwd_topology_tx_port_get()
4019 return rxp; in fwd_topology_tx_port_get()
4064 portid_t rxp; in rss_fwd_config_setup() local
4101 rxp = 0; in rss_fwd_config_setup()
4114 rxp++; in rss_fwd_config_setup()
4117 rxp = 0; in rss_fwd_config_setup()
4244 rxp++; in dcb_fwd_config_setup()
4260 portid_t rxp; in icmp_echo_config_setup() local
4287 rxp = 0; rxq = 0; in icmp_echo_config_setup()
[all …]
H A Dtestpmd.c2150 portid_t rxp; in flush_fwd_rx_queues() local
2168 for (rxp = 0; rxp < cur_fwd_config.nb_fwd_ports; rxp++) { in flush_fwd_rx_queues()
2170 port_id = fwd_ports_ids[rxp]; in flush_fwd_rx_queues()