]>
git.proxmox.com Git - ceph.git/blob - ceph/src/dpdk/lib/librte_eal/common/include/arch/arm/rte_vect.h
4 * Copyright(c) 2015 Cavium Networks. All rights reserved.
6 * Redistribution and use in source and binary forms, with or without
7 * modification, are permitted provided that the following conditions
10 * * Redistributions of source code must retain the above copyright
11 * notice, this list of conditions and the following disclaimer.
12 * * Redistributions in binary form must reproduce the above copyright
13 * notice, this list of conditions and the following disclaimer in
14 * the documentation and/or other materials provided with the
16 * * Neither the name of Cavium Networks nor the names of its
17 * contributors may be used to endorse or promote products derived
18 * from this software without specific prior written permission.
20 * THIS SOFTWARE IS PROVIDED BY THE COPYRIGHT HOLDERS AND CONTRIBUTORS
21 * "AS IS" AND ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT
22 * LIMITED TO, THE IMPLIED WARRANTIES OF MERCHANTABILITY AND FITNESS FOR
23 * A PARTICULAR PURPOSE ARE DISCLAIMED. IN NO EVENT SHALL THE COPYRIGHT
24 * OWNER OR CONTRIBUTORS BE LIABLE FOR ANY DIRECT, INDIRECT, INCIDENTAL,
25 * SPECIAL, EXEMPLARY, OR CONSEQUENTIAL DAMAGES (INCLUDING, BUT NOT
26 * LIMITED TO, PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE,
27 * DATA, OR PROFITS; OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY
28 * THEORY OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT
29 * (INCLUDING NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE
30 * OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
33 #ifndef _RTE_VECT_ARM_H_
34 #define _RTE_VECT_ARM_H_
43 typedef int32x4_t xmm_t
;
45 #define XMM_SIZE (sizeof(xmm_t))
46 #define XMM_MASK (XMM_SIZE - 1)
48 typedef union rte_xmm
{
50 uint8_t u8
[XMM_SIZE
/ sizeof(uint8_t)];
51 uint16_t u16
[XMM_SIZE
/ sizeof(uint16_t)];
52 uint32_t u32
[XMM_SIZE
/ sizeof(uint32_t)];
53 uint64_t u64
[XMM_SIZE
/ sizeof(uint64_t)];
54 double pd
[XMM_SIZE
/ sizeof(double)];
55 } __attribute__((aligned(16))) rte_xmm_t
;
58 /* NEON intrinsic vqtbl1q_u8() is not supported in ARMv7-A(AArch32) */
59 static __inline uint8x16_t
60 vqtbl1q_u8(uint8x16_t a
, uint8x16_t b
)
63 rte_xmm_t rte_a
, rte_b
, rte_ret
;
65 vst1q_u8(rte_a
.u8
, a
);
66 vst1q_u8(rte_b
.u8
, b
);
68 for (i
= 0; i
< 16; i
++) {
71 rte_ret
.u8
[i
] = rte_a
.u8
[pos
];
76 return vld1q_u8(rte_ret
.u8
);