git.droids-corp.org
/
dpdk.git
/ blobdiff
commit
grep
author
committer
pickaxe
?
search:
re
summary
|
shortlog
|
log
|
commit
|
commitdiff
|
tree
raw
|
inline
| side by side
doc: announce dpaa-specific API parameter change
[dpdk.git]
/
drivers
/
net
/
i40e
/
i40e_rxtx_vec_neon.c
diff --git
a/drivers/net/i40e/i40e_rxtx_vec_neon.c
b/drivers/net/i40e/i40e_rxtx_vec_neon.c
index
d7d6dec
..
6f874e4
100644
(file)
--- a/
drivers/net/i40e/i40e_rxtx_vec_neon.c
+++ b/
drivers/net/i40e/i40e_rxtx_vec_neon.c
@@
-6,6
+6,7
@@
#include <stdint.h>
#include <rte_ethdev_driver.h>
#include <rte_malloc.h>
#include <stdint.h>
#include <rte_ethdev_driver.h>
#include <rte_malloc.h>
+#include <rte_vect.h>
#include "base/i40e_prototype.h"
#include "base/i40e_type.h"
#include "base/i40e_prototype.h"
#include "base/i40e_type.h"
@@
-13,7
+14,6
@@
#include "i40e_rxtx.h"
#include "i40e_rxtx_vec_common.h"
#include "i40e_rxtx.h"
#include "i40e_rxtx_vec_common.h"
-#include <arm_neon.h>
#pragma GCC diagnostic ignored "-Wcast-qual"
#pragma GCC diagnostic ignored "-Wcast-qual"
@@
-72,8
+72,9
@@
i40e_rxq_rearm(struct i40e_rx_queue *rxq)
rx_id = (uint16_t)((rxq->rxrearm_start == 0) ?
(rxq->nb_rx_desc - 1) : (rxq->rxrearm_start - 1));
rx_id = (uint16_t)((rxq->rxrearm_start == 0) ?
(rxq->nb_rx_desc - 1) : (rxq->rxrearm_start - 1));
+ rte_cio_wmb();
/* Update the tail pointer on the NIC */
/* Update the tail pointer on the NIC */
- I40E_PCI_REG_WRITE(rxq->qrx_tail, rx_id);
+ I40E_PCI_REG_WRITE
_RELAXED
(rxq->qrx_tail, rx_id);
}
static inline void
}
static inline void
@@
-171,8
+172,8
@@
desc_to_olflags_v(struct i40e_rx_queue *rxq, uint64x2_t descs[4],
#define I40E_UINT16_BIT (CHAR_BIT * sizeof(uint16_t))
static inline void
#define I40E_UINT16_BIT (CHAR_BIT * sizeof(uint16_t))
static inline void
-desc_to_ptype_v(uint64x2_t descs[4], struct rte_mbuf **rx_pkts,
- uint32_t *ptype_tbl)
+desc_to_ptype_v(uint64x2_t descs[4], struct rte_mbuf **
__rte_restrict
rx_pkts,
+ uint32_t *
__rte_restrict
ptype_tbl)
{
int i;
uint8_t ptype;
{
int i;
uint8_t ptype;
@@
-193,7
+194,8
@@
desc_to_ptype_v(uint64x2_t descs[4], struct rte_mbuf **rx_pkts,
* numbers of DD bits
*/
static inline uint16_t
* numbers of DD bits
*/
static inline uint16_t
-_recv_raw_pkts_vec(struct i40e_rx_queue *rxq, struct rte_mbuf **rx_pkts,
+_recv_raw_pkts_vec(struct i40e_rx_queue *__rte_restrict rxq,
+ struct rte_mbuf **__rte_restrict rx_pkts,
uint16_t nb_pkts, uint8_t *split_packet)
{
volatile union i40e_rx_desc *rxdp;
uint16_t nb_pkts, uint8_t *split_packet)
{
volatile union i40e_rx_desc *rxdp;
@@
-431,8
+433,8
@@
_recv_raw_pkts_vec(struct i40e_rx_queue *rxq, struct rte_mbuf **rx_pkts,
* numbers of DD bits
*/
uint16_t
* numbers of DD bits
*/
uint16_t
-i40e_recv_pkts_vec(void *
rx_queue, struct rte_mbuf **rx_pkts
,
-
uint16_t nb_pkts)
+i40e_recv_pkts_vec(void *
__rte_restrict rx_queue
,
+
struct rte_mbuf **__rte_restrict rx_pkts,
uint16_t nb_pkts)
{
return _recv_raw_pkts_vec(rx_queue, rx_pkts, nb_pkts, NULL);
}
{
return _recv_raw_pkts_vec(rx_queue, rx_pkts, nb_pkts, NULL);
}
@@
-493,8
+495,8
@@
vtx1(volatile struct i40e_tx_desc *txdp,
}
static inline void
}
static inline void
-vtx(volatile struct i40e_tx_desc *txdp,
-
struct rte_mbuf **pkt,
uint16_t nb_pkts, uint64_t flags)
+vtx(volatile struct i40e_tx_desc *txdp,
struct rte_mbuf **pkt,
+ uint16_t nb_pkts, uint64_t flags)
{
int i;
{
int i;
@@
-503,8
+505,8
@@
vtx(volatile struct i40e_tx_desc *txdp,
}
uint16_t
}
uint16_t
-i40e_xmit_fixed_burst_vec(void *
tx_queue, struct rte_mbuf **tx_pkts
,
-
uint16_t nb_pkts)
+i40e_xmit_fixed_burst_vec(void *
__rte_restrict tx_queue
,
+
struct rte_mbuf **__rte_restrict tx_pkts,
uint16_t nb_pkts)
{
struct i40e_tx_queue *txq = (struct i40e_tx_queue *)tx_queue;
volatile struct i40e_tx_desc *txdp;
{
struct i40e_tx_queue *txq = (struct i40e_tx_queue *)tx_queue;
volatile struct i40e_tx_desc *txdp;
@@
-564,7
+566,8
@@
i40e_xmit_fixed_burst_vec(void *tx_queue, struct rte_mbuf **tx_pkts,
txq->tx_tail = tx_id;
txq->tx_tail = tx_id;
- I40E_PCI_REG_WRITE(txq->qtx_tail, txq->tx_tail);
+ rte_cio_wmb();
+ I40E_PCI_REG_WRITE_RELAXED(txq->qtx_tail, tx_id);
return nb_pkts;
}
return nb_pkts;
}