3ee2304b51fff2012907e46391fe7033e5476a27
[dpdk.git] / examples / l3fwd / l3fwd_em_hlm_neon.h
1 /* SPDX-License-Identifier: BSD-3-Clause
2  * Copyright(c) 2016-2018 Intel Corporation.
3  * Copyright(c) 2017-2018 Linaro Limited.
4  */
5
6 #ifndef __L3FWD_EM_HLM_NEON_H__
7 #define __L3FWD_EM_HLM_NEON_H__
8
9 #include <arm_neon.h>
10
11 static inline void
12 get_ipv4_5tuple(struct rte_mbuf *m0, int32x4_t mask0,
13                 union ipv4_5tuple_host *key)
14 {
15         int32x4_t tmpdata0 = vld1q_s32(rte_pktmbuf_mtod_offset(m0, int32_t *,
16                                 sizeof(struct rte_ether_hdr) +
17                                 offsetof(struct ipv4_hdr, time_to_live)));
18
19         key->xmm = vandq_s32(tmpdata0, mask0);
20 }
21
22 static inline void
23 get_ipv6_5tuple(struct rte_mbuf *m0, int32x4_t mask0,
24                 int32x4_t mask1, union ipv6_5tuple_host *key)
25 {
26         int32x4_t tmpdata0 = vld1q_s32(
27                         rte_pktmbuf_mtod_offset(m0, int *,
28                                 sizeof(struct rte_ether_hdr) +
29                                 offsetof(struct ipv6_hdr, payload_len)));
30
31         int32x4_t tmpdata1 = vld1q_s32(
32                         rte_pktmbuf_mtod_offset(m0, int *,
33                                 sizeof(struct rte_ether_hdr) +
34                                 offsetof(struct ipv6_hdr, payload_len) + 8));
35
36         int32x4_t tmpdata2 = vld1q_s32(
37                         rte_pktmbuf_mtod_offset(m0, int *,
38                                 sizeof(struct rte_ether_hdr) +
39                                 offsetof(struct ipv6_hdr, payload_len) + 16));
40
41         key->xmm[0] = vandq_s32(tmpdata0, mask0);
42         key->xmm[1] = tmpdata1;
43         key->xmm[2] = vandq_s32(tmpdata2, mask1);
44 }
45 #endif /* __L3FWD_EM_HLM_NEON_H__ */