blob: ce1b9a554e5f793c46c11719b732551f757d1ae6 [file] [log] [blame]
Georgios Pinitas82833b82018-01-30 12:14:24 +00001/*
Omar Al Khatib605a9282022-11-01 17:01:24 +00002 * Copyright (c) 2018-2020, 2022 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 */
Michalis Spyrouf4643372019-11-29 16:17:13 +000024#ifndef ARM_COMPUTE_WRAPPER_STORE_H
25#define ARM_COMPUTE_WRAPPER_STORE_H
Georgios Pinitas82833b82018-01-30 12:14:24 +000026
Georgios Pinitas82833b82018-01-30 12:14:24 +000027#include <arm_neon.h>
28
29namespace arm_compute
30{
31namespace wrapper
32{
33#define VSTORE_IMPL(stype, vtype, prefix, postfix) \
34 inline void vstore(stype *ptr, vtype val) \
35 { \
36 prefix##_##postfix(ptr, val); \
37 }
38
39VSTORE_IMPL(uint8_t, uint8x8_t, vst1, u8)
Manuel Bottinib4bb8272019-12-18 18:01:27 +000040VSTORE_IMPL(uint8_t, uint8x8x2_t, vst2, u8)
Georgios Pinitas82833b82018-01-30 12:14:24 +000041VSTORE_IMPL(int8_t, int8x8_t, vst1, s8)
Manuel Bottinib4bb8272019-12-18 18:01:27 +000042VSTORE_IMPL(int8_t, int8x8x2_t, vst2, s8)
Georgios Pinitas82833b82018-01-30 12:14:24 +000043VSTORE_IMPL(uint16_t, uint16x4_t, vst1, u16)
44VSTORE_IMPL(int16_t, int16x4_t, vst1, s16)
45VSTORE_IMPL(uint32_t, uint32x2_t, vst1, u32)
46VSTORE_IMPL(int32_t, int32x2_t, vst1, s32)
Georgios Pinitas82833b82018-01-30 12:14:24 +000047VSTORE_IMPL(float, float32x2_t, vst1, f32)
Michalis Spyroubcf8a962018-10-12 10:51:31 +010048#ifdef __ARM_FEATURE_FP16_VECTOR_ARITHMETIC
49VSTORE_IMPL(float16_t, float16x4_t, vst1, f16)
50#endif // __ARM_FEATURE_FP16_VECTOR_ARITHMETIC
Georgios Pinitas82833b82018-01-30 12:14:24 +000051
52VSTORE_IMPL(uint8_t, uint8x16_t, vst1q, u8)
53VSTORE_IMPL(int8_t, int8x16_t, vst1q, s8)
54VSTORE_IMPL(uint16_t, uint16x8_t, vst1q, u16)
55VSTORE_IMPL(int16_t, int16x8_t, vst1q, s16)
56VSTORE_IMPL(uint32_t, uint32x4_t, vst1q, u32)
57VSTORE_IMPL(int32_t, int32x4_t, vst1q, s32)
Georgios Pinitas82833b82018-01-30 12:14:24 +000058VSTORE_IMPL(float, float32x4_t, vst1q, f32)
Michalis Spyroubcf8a962018-10-12 10:51:31 +010059#ifdef __ARM_FEATURE_FP16_VECTOR_ARITHMETIC
60VSTORE_IMPL(float16_t, float16x8_t, vst1q, f16)
61#endif // __ARM_FEATURE_FP16_VECTOR_ARITHMETIC
Georgios Pinitas57c033b2018-02-15 12:29:44 +000062
63#undef VSTORE_IMPL
64} // namespace wrapper
65} // namespace arm_compute
Michalis Spyrouf4643372019-11-29 16:17:13 +000066#endif /* ARM_COMPUTE_WRAPPER_STORE_H */