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
8b99354
..
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"
@@
-172,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;
@@
-194,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;
@@
-432,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);
}
@@
-494,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;
@@
-504,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;