]>
git.proxmox.com Git - ceph.git/blob - ceph/src/spdk/dpdk/lib/librte_eal/common/include/arch/x86/rte_vect.h
1 /* SPDX-License-Identifier: BSD-3-Clause
2 * Copyright(c) 2010-2015 Intel Corporation
5 #ifndef _RTE_VECT_X86_H_
6 #define _RTE_VECT_X86_H_
11 * RTE SSE/AVX related header.
15 #include <rte_config.h>
16 #include "generic/rte_vect.h"
18 #if (defined(__ICC) || (__GNUC__ == 4 && __GNUC_MINOR__ < 4))
20 #include <smmintrin.h> /* SSE4 */
23 #include <immintrin.h>
28 #include <x86intrin.h>
36 typedef __m128i xmm_t
;
38 #define XMM_SIZE (sizeof(xmm_t))
39 #define XMM_MASK (XMM_SIZE - 1)
41 typedef union rte_xmm
{
43 uint8_t u8
[XMM_SIZE
/ sizeof(uint8_t)];
44 uint16_t u16
[XMM_SIZE
/ sizeof(uint16_t)];
45 uint32_t u32
[XMM_SIZE
/ sizeof(uint32_t)];
46 uint64_t u64
[XMM_SIZE
/ sizeof(uint64_t)];
47 double pd
[XMM_SIZE
/ sizeof(double)];
52 typedef __m256i ymm_t
;
54 #define YMM_SIZE (sizeof(ymm_t))
55 #define YMM_MASK (YMM_SIZE - 1)
57 typedef union rte_ymm
{
59 xmm_t x
[YMM_SIZE
/ sizeof(xmm_t
)];
60 uint8_t u8
[YMM_SIZE
/ sizeof(uint8_t)];
61 uint16_t u16
[YMM_SIZE
/ sizeof(uint16_t)];
62 uint32_t u32
[YMM_SIZE
/ sizeof(uint32_t)];
63 uint64_t u64
[YMM_SIZE
/ sizeof(uint64_t)];
64 double pd
[YMM_SIZE
/ sizeof(double)];
70 #define _mm_cvtsi128_si64(a) \
79 * Prior to version 12.1 icc doesn't support _mm_set_epi64x.
81 #if (defined(__ICC) && __ICC < 1210)
82 #define _mm_set_epi64x(a, b) \
89 #endif /* (defined(__ICC) && __ICC < 1210) */
95 #endif /* _RTE_VECT_X86_H_ */