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
eal/armv7: emulate vaddvq u16 variant
[dpdk.git]
/
lib
/
librte_eal
/
common
/
include
/
arch
/
arm
/
rte_vect.h
diff --git
a/lib/librte_eal/common/include/arch/arm/rte_vect.h
b/lib/librte_eal/common/include/arch/arm/rte_vect.h
index
ea7be29
..
7fec25e
100644
(file)
--- a/
lib/librte_eal/common/include/arch/arm/rte_vect.h
+++ b/
lib/librte_eal/common/include/arch/arm/rte_vect.h
@@
-77,6
+77,17
@@
vqtbl1q_u8(uint8x16_t a, uint8x16_t b)
return vld1q_u8(rte_ret.u8);
}
return vld1q_u8(rte_ret.u8);
}
+
+static inline uint16_t
+vaddvq_u16(uint16x8_t a)
+{
+ uint32x4_t m = vpaddlq_u16(a);
+ uint64x2_t n = vpaddlq_u32(m);
+ uint64x1_t o = vget_low_u64(n) + vget_high_u64(n);
+
+ return vget_lane_u32((uint32x2_t)o, 0);
+}
+
#endif
#if defined(RTE_TOOLCHAIN_GCC) && (GCC_VERSION < 70000)
#endif
#if defined(RTE_TOOLCHAIN_GCC) && (GCC_VERSION < 70000)