blob: 1dac61af74382cf6f8576b64608fc20dc1b1ac36 [file] [log] [blame]
Georgios Pinitas82833b82018-01-30 12:14:24 +00001/*
Gunes Bayirc0713282023-09-14 15:14:48 +01002 * Copyright (c) 2018-2021, 2023 Arm Limited.
Georgios Pinitas82833b82018-01-30 12:14:24 +00003 *
4 * SPDX-License-Identifier: MIT
5 *
6 * Permission is hereby granted, free of charge, to any person obtaining a copy
7 * of this software and associated documentation files (the "Software"), to
8 * deal in the Software without restriction, including without limitation the
9 * rights to use, copy, modify, merge, publish, distribute, sublicense, and/or
10 * sell copies of the Software, and to permit persons to whom the Software is
11 * furnished to do so, subject to the following conditions:
12 *
13 * The above copyright notice and this permission notice shall be included in all
14 * copies or substantial portions of the Software.
15 *
16 * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
17 * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
18 * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE
19 * AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
20 * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
21 * OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN THE
22 * SOFTWARE.
23 */
Gunes Bayirc0713282023-09-14 15:14:48 +010024#ifndef ACL_SRC_CORE_NEON_WRAPPER_TRAITS_H
25#define ACL_SRC_CORE_NEON_WRAPPER_TRAITS_H
26
27#include "arm_compute/core/CoreTypes.h"
28
29#if defined(__ARM_FEATURE_FP16_VECTOR_ARITHMETIC)
30#include "src/cpu/CpuTypes.h" // required for float16_t
31#endif // defined(__ARM_FEATURE_FP16_VECTOR_ARITHMETIC)
Georgios Pinitas82833b82018-01-30 12:14:24 +000032
33#include <arm_neon.h>
34
Viet-Hoa Dobcf95522023-11-01 11:27:32 +000035#if defined(ARM_COMPUTE_ENABLE_SVE) && defined(__ARM_FEATURE_SVE)
Michalis Spyroub5a450a2021-01-06 17:40:30 +000036#include <arm_sve.h>
Viet-Hoa Dobcf95522023-11-01 11:27:32 +000037#endif /* defined(ARM_COMPUTE_ENABLE_SVE) && defined(__ARM_FEATURE_SVE) */
Michalis Spyroub5a450a2021-01-06 17:40:30 +000038
Gunes Bayirc0713282023-09-14 15:14:48 +010039#include <cmath>
40#include <cstdint>
41
Georgios Pinitas82833b82018-01-30 12:14:24 +000042namespace arm_compute
43{
44namespace wrapper
45{
46namespace traits
47{
48// *INDENT-OFF*
49// clang-format off
50
Georgios Pinitas57c033b2018-02-15 12:29:44 +000051/** 64-bit vector tag */
52struct vector_64_tag {};
53/** 128-bit vector tag */
54struct vector_128_tag {};
55
Michele Di Giorgio33f41fa2021-03-09 14:09:08 +000056/** Create the appropriate SIMD vector given its type and size in terms of elements */
Georgios Pinitas82833b82018-01-30 12:14:24 +000057template <typename T, int S> struct neon_vector;
Manuel Bottinib4bb8272019-12-18 18:01:27 +000058
Alex Gildayc357c472018-03-21 13:54:09 +000059// Specializations
60#ifndef DOXYGEN_SKIP_THIS
giuros01d5134362019-05-14 16:12:53 +010061template <> struct neon_vector<uint8_t, 8>{ using scalar_type = uint8_t; using type = uint8x8_t; using tag_type = vector_64_tag; };
62template <> struct neon_vector<int8_t, 8>{ using scalar_type = int8_t; using type = int8x8_t; using tag_type = vector_64_tag; };
63template <> struct neon_vector<uint8_t, 16>{ using scalar_type = uint8_t; using type = uint8x16_t; using tag_type = vector_128_tag; };
64template <> struct neon_vector<int8_t, 16>{ using scalar_type = int8_t; using type = int8x16_t; using tag_type = vector_128_tag; };
65template <> struct neon_vector<uint16_t, 4>{ using scalar_type = uint16_t; using type = uint16x4_t; using tag_type = vector_64_tag; };
66template <> struct neon_vector<int16_t, 4>{ using scalar_type = int16_t; using type = int16x4_t; using tag_type = vector_64_tag; };
67template <> struct neon_vector<uint16_t, 8>{ using scalar_type = uint16_t; using type = uint16x8_t; using tag_type = vector_128_tag; };
Manuel Bottinib4bb8272019-12-18 18:01:27 +000068template <> struct neon_vector<uint16_t, 16>{ using scalar_type = uint16_t; using type = uint16x8x2_t; };
giuros01d5134362019-05-14 16:12:53 +010069template <> struct neon_vector<int16_t, 8>{ using scalar_type = int16_t; using type = int16x8_t; using tag_type = vector_128_tag; };
Manuel Bottinib4bb8272019-12-18 18:01:27 +000070template <> struct neon_vector<int16_t, 16>{ using scalar_type = int16_t; using type = int16x8x2_t; };
giuros01d5134362019-05-14 16:12:53 +010071template <> struct neon_vector<uint32_t, 2>{ using scalar_type = uint32_t; using type = uint32x2_t; using tag_type = vector_64_tag; };
72template <> struct neon_vector<int32_t, 2>{ using scalar_type = int32_t; using type = int32x2_t; using tag_type = vector_64_tag; };
73template <> struct neon_vector<uint32_t, 4>{ using scalar_type = uint32_t; using type = uint32x4_t; using tag_type = vector_128_tag; };
74template <> struct neon_vector<int32_t, 4>{ using scalar_type = int32_t; using type = int32x4_t; using tag_type = vector_128_tag; };
75template <> struct neon_vector<uint64_t, 1>{ using scalar_type = uint64_t;using type = uint64x1_t; using tag_type = vector_64_tag; };
76template <> struct neon_vector<int64_t, 1>{ using scalar_type = int64_t; using type = int64x1_t; using tag_type = vector_64_tag; };
77template <> struct neon_vector<uint64_t, 2>{ using scalar_type = uint64_t; using type = uint64x2_t; using tag_type = vector_128_tag; };
78template <> struct neon_vector<int64_t, 2>{ using scalar_type = int64_t; using type = int64x2_t; using tag_type = vector_128_tag; };
79template <> struct neon_vector<float_t, 2>{ using scalar_type = float_t; using type = float32x2_t; using tag_type = vector_64_tag; };
80template <> struct neon_vector<float_t, 4>{ using scalar_type = float_t; using type = float32x4_t; using tag_type = vector_128_tag; };
Manuel Bottinib4bb8272019-12-18 18:01:27 +000081
Georgios Pinitasaaba4c62018-08-22 16:20:21 +010082#ifdef __ARM_FEATURE_FP16_VECTOR_ARITHMETIC
giuros01d5134362019-05-14 16:12:53 +010083template <> struct neon_vector<float16_t, 4>{ using scalar_type = float16_t; using type = float16x4_t; using tag_type = vector_64_tag; };
84template <> struct neon_vector<float16_t, 8>{ using scalar_type = float16_t; using type = float16x8_t; using tag_type = vector_128_tag; };
Georgios Pinitasaaba4c62018-08-22 16:20:21 +010085#endif // __ARM_FEATURE_FP16_VECTOR_ARITHMETIC
Alex Gildayc357c472018-03-21 13:54:09 +000086#endif /* DOXYGEN_SKIP_THIS */
Georgios Pinitas57c033b2018-02-15 12:29:44 +000087
88/** Helper type template to get the type of a neon vector */
Georgios Pinitas82833b82018-01-30 12:14:24 +000089template <typename T, int S> using neon_vector_t = typename neon_vector<T, S>::type;
Georgios Pinitas57c033b2018-02-15 12:29:44 +000090/** Helper type template to get the tag type of a neon vector */
91template <typename T, int S> using neon_vector_tag_t = typename neon_vector<T, S>::tag_type;
Georgios Pinitas52ebf422018-12-17 18:21:02 +000092
93/** Vector bit-width enum class */
94enum class BitWidth
95{
96 W64, /**< 64-bit width */
97 W128, /**< 128-bit width */
98};
99
Michele Di Giorgio33f41fa2021-03-09 14:09:08 +0000100/** Create the appropriate SIMD vector given its type and size in terms of bits */
Georgios Pinitas52ebf422018-12-17 18:21:02 +0000101template <typename T, BitWidth BW> struct neon_bitvector;
102// Specializations
103#ifndef DOXYGEN_SKIP_THIS
104template <> struct neon_bitvector<uint8_t, BitWidth::W64>{ using type = uint8x8_t; using tag_type = vector_64_tag; };
105template <> struct neon_bitvector<int8_t, BitWidth::W64>{ using type = int8x8_t; using tag_type = vector_64_tag; };
106template <> struct neon_bitvector<uint8_t, BitWidth::W128>{ using type = uint8x16_t; using tag_type = vector_128_tag; };
107template <> struct neon_bitvector<int8_t, BitWidth::W128>{ using type = int8x16_t; using tag_type = vector_128_tag; };
108template <> struct neon_bitvector<uint16_t, BitWidth::W64>{ using type = uint16x4_t; using tag_type = vector_64_tag; };
109template <> struct neon_bitvector<int16_t, BitWidth::W64>{ using type = int16x4_t; using tag_type = vector_64_tag; };
110template <> struct neon_bitvector<uint16_t, BitWidth::W128>{ using type = uint16x8_t; using tag_type = vector_128_tag; };
111template <> struct neon_bitvector<int16_t, BitWidth::W128>{ using type = int16x8_t; using tag_type = vector_128_tag; };
112template <> struct neon_bitvector<uint32_t, BitWidth::W64>{ using type = uint32x2_t; using tag_type = vector_64_tag; };
113template <> struct neon_bitvector<int32_t, BitWidth::W64>{ using type = int32x2_t; using tag_type = vector_64_tag; };
114template <> struct neon_bitvector<uint32_t, BitWidth::W128>{ using type = uint32x4_t; using tag_type = vector_128_tag; };
115template <> struct neon_bitvector<int32_t, BitWidth::W128>{ using type = int32x4_t; using tag_type = vector_128_tag; };
116template <> struct neon_bitvector<uint64_t, BitWidth::W64>{ using type = uint64x1_t; using tag_type = vector_64_tag; };
117template <> struct neon_bitvector<int64_t, BitWidth::W64>{ using type = int64x1_t; using tag_type = vector_64_tag; };
118template <> struct neon_bitvector<uint64_t, BitWidth::W128>{ using type = uint64x2_t; using tag_type = vector_128_tag; };
119template <> struct neon_bitvector<int64_t, BitWidth::W128>{ using type = int64x2_t; using tag_type = vector_128_tag; };
120template <> struct neon_bitvector<float_t, BitWidth::W64>{ using type = float32x2_t; using tag_type = vector_64_tag; };
121template <> struct neon_bitvector<float_t, BitWidth::W128>{ using type = float32x4_t; using tag_type = vector_128_tag; };
122#ifdef __ARM_FEATURE_FP16_VECTOR_ARITHMETIC
123template <> struct neon_bitvector<float16_t, BitWidth::W64>{ using type = float16x4_t; using tag_type = vector_64_tag; };
124template <> struct neon_bitvector<float16_t, BitWidth::W128>{ using type = float16x8_t; using tag_type = vector_128_tag; };
125#endif // __ARM_FEATURE_FP16_VECTOR_ARITHMETIC
Michalis Spyroub5a450a2021-01-06 17:40:30 +0000126
127
Viet-Hoa Dobcf95522023-11-01 11:27:32 +0000128#if defined(ARM_COMPUTE_ENABLE_SVE) && defined(__ARM_FEATURE_SVE)
Michalis Spyroub5a450a2021-01-06 17:40:30 +0000129/** Create the appropriate SVE vector given its type */
130template <typename T> struct sve_vector;
131
132template <> struct sve_vector<uint8_t>{ using scalar_type = uint8_t; using type = svuint8_t; };
133template <> struct sve_vector<int8_t>{ using scalar_type = int8_t; using type = svint8_t; };
Viet-Hoa Dobcf95522023-11-01 11:27:32 +0000134#endif /* defined(ARM_COMPUTE_ENABLE_SVE) && defined(__ARM_FEATURE_SVE) */
Michalis Spyroub5a450a2021-01-06 17:40:30 +0000135
Georgios Pinitas52ebf422018-12-17 18:21:02 +0000136#endif /* DOXYGEN_SKIP_THIS */
137
138/** Helper type template to get the type of a neon vector */
139template <typename T, BitWidth BW> using neon_bitvector_t = typename neon_bitvector<T, BW>::type;
140/** Helper type template to get the tag type of a neon vector */
141template <typename T, BitWidth BW> using neon_bitvector_tag_t = typename neon_bitvector<T, BW>::tag_type;
Georgios Pinitasdbdea0d2019-10-16 19:21:40 +0100142
143/** Promote a type */
144template <typename T> struct promote { };
145template <> struct promote<uint8_t> { using type = uint16_t; };
146template <> struct promote<int8_t> { using type = int16_t; };
147template <> struct promote<uint16_t> { using type = uint32_t; };
148template <> struct promote<int16_t> { using type = int32_t; };
149template <> struct promote<uint32_t> { using type = uint64_t; };
150template <> struct promote<int32_t> { using type = int64_t; };
151template <> struct promote<float> { using type = float; };
152template <> struct promote<half> { using type = half; };
153
154/** Get promoted type */
155template <typename T>
156using promote_t = typename promote<T>::type;
157
Georgios Pinitas82833b82018-01-30 12:14:24 +0000158// clang-format on
159// *INDENT-ON*
Georgios Pinitas57c033b2018-02-15 12:29:44 +0000160} // namespace traits
161} // namespace wrapper
162} // namespace arm_compute
Gunes Bayirc0713282023-09-14 15:14:48 +0100163#endif // ACL_SRC_CORE_NEON_WRAPPER_TRAITS_H