diff options
Diffstat (limited to 'src/core/NEON/SVEMath.h')
| -rw-r--r-- | src/core/NEON/SVEMath.h | 248 |
1 files changed, 248 insertions, 0 deletions
diff --git a/src/core/NEON/SVEMath.h b/src/core/NEON/SVEMath.h new file mode 100644 index 0000000000..49ed9df720 --- /dev/null +++ b/src/core/NEON/SVEMath.h @@ -0,0 +1,248 @@ +/* + * Copyright (c) 2020-2021, 2023 Arm Limited. + * + * SPDX-License-Identifier: MIT + * + * Permission is hereby granted, free of charge, to any person obtaining a copy + * of this software and associated documentation files (the "Software"), to + * deal in the Software without restriction, including without limitation the + * rights to use, copy, modify, merge, publish, distribute, sublicense, and/or + * sell copies of the Software, and to permit persons to whom the Software is + * furnished to do so, subject to the following conditions: + * + * The above copyright notice and this permission notice shall be included in all + * copies or substantial portions of the Software. + * + * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR + * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY, + * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE + * AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER + * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM, + * OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN THE + * SOFTWARE. + */ +#ifndef ACL_SRC_CORE_NEON_SVEMATH_H +#define ACL_SRC_CORE_NEON_SVEMATH_H + +#if defined(ARM_COMPUTE_ENABLE_SVE) +#include "src/core/NEON/wrapper/intrinsics/svcvt.h" +#include "src/core/NEON/wrapper/intrinsics/svdup_n.h" +#include "src/core/NEON/wrapper/intrinsics/svreinterpret.h" + +#include <arm_sve.h> +#include <array> + +namespace arm_compute +{ +/** Calculate exponent. + * + * @param[in] pg Input predicate. + * @param[in] val Input vector value in F32 format. + * + * @return The calculated exponent. + */ +svfloat32_t svexp_f32_z(svbool_t pg, svfloat32_t val); + +/** Calculate reciprocal. + * + * @param[in] pg Input predicate. + * @param[in] x Input value. + * + * @return The calculated reciprocal. + */ +svfloat32_t svinv_f32_z(svbool_t pg, svfloat32_t x); + +/** Calculate logarithm + * + * @param[in] pg Input predicate. + * @param[in] x Input vector value in F32 format. + * + * @return The calculated logarithm. + */ +svfloat32_t svlog_f32_z(svbool_t pg, svfloat32_t x); + +/** Calculate hyperbolic tangent. + * + * tanh(x) = (e^2x - 1)/(e^2x + 1) + * + * @note We clamp x to [-5,5] to avoid overflowing issues. + * + * @param[in] pg Input predicate. + * @param[in] val Input vector value in F32 format. + * + * @return The calculated Hyperbolic Tangent. + */ +svfloat32_t svtanh_f32_z(svbool_t pg, svfloat32_t val); + +/** Calculate hyperbolic tangent. + * + * tanh(x) = (e^2x - 1)/(e^2x + 1) + * + * @note We clamp x to [-5,5] to avoid overflowing issues. + * + * @param[in] pg Input predicate. + * @param[in] val Input vector value in F16 format. + * + * @return The calculated Hyperbolic Tangent. + */ +svfloat16_t svtanh_f16_z(svbool_t pg, svfloat16_t val); + +/** Calculate exponential + * + * @param[in] pg Input predicate. + * @param[in] x Input vector value in F16 format. + * + * @return The calculated exponent. + */ +svfloat16_t svexp_f16_z(svbool_t pg, svfloat16_t x); + +#ifdef ARM_COMPUTE_ENABLE_SVE2 + +/** Calculate exponential + * + * @param[in] pg Input predicate. + * @param[in] x Input vector value in F16 format. + * + * @return The calculated exponent. + */ +svfloat16_t svexp_f16_z_sve2(svbool_t pg, svfloat16_t x); + +#endif // ARM_COMPUTE_ENABLE_SVE2 + +/** Calculate reciprocal. + * + * @param[in] pg Input predicate. + * @param[in] x Input value. + * + * @return The calculated reciprocal. + */ +svfloat16_t svinv_f16_z(svbool_t pg, svfloat16_t x); + +/** Calculate logarithm + * + * @param[in] pg Input predicate. + * @param[in] x Input vector value in F32 format. + * + * @return The calculated logarithm. + */ +svfloat16_t svlog_f16_z(svbool_t pg, svfloat16_t x); + +#ifdef ARM_COMPUTE_ENABLE_SVE2 + +/** Calculate logarithm + * + * @param[in] pg Input predicate. + * @param[in] x Input vector value in F32 format. + * + * @return The calculated logarithm. + */ +svfloat16_t svlog_f16_z_sve2(svbool_t pg, svfloat16_t x); + +#endif // ARM_COMPUTE_ENABLE_SVE2 + +/** Calculate inverse square root. + * + * @param[in] pg Input predicate. + * @param[in] val Input value. + * + * @return The calculated inverse square root. + */ +template <typename VectorType> +inline VectorType svinvsqrt(svbool_t pg, VectorType val) +{ + auto sqrt_reciprocal = svrsqrte(val); + sqrt_reciprocal = svmul_z(pg, svrsqrts(svmul_z(pg, val, sqrt_reciprocal), sqrt_reciprocal), sqrt_reciprocal); + sqrt_reciprocal = svmul_z(pg, svrsqrts(svmul_z(pg, val, sqrt_reciprocal), sqrt_reciprocal), sqrt_reciprocal); + return sqrt_reciprocal; +} + +/** Calculate sine. + * + * @param[in] pg Input predicate. + * @param[in] val Input vector value in radians, F32 format. + * + * @return The calculated sine. + */ +svfloat32_t svsin_f32_z(svbool_t pg, svfloat32_t val); + +/** Calculate sine. + * + * @param[in] pg Input predicate. + * @param[in] val Input vector value in radians, F16 format. + * + * @return The calculated sine. + */ +svfloat16_t svsin_f16_z(svbool_t pg, svfloat16_t val); + +#ifdef ARM_COMPUTE_ENABLE_SVE2 + +/** Calculate sine. + * + * @param[in] pg Input predicate. + * @param[in] val Input vector value in radians, F16 format. + * + * @return The calculated sine. + */ +svfloat16_t svsin_f16_z_sve2(svbool_t pg, svfloat16_t val); + +#endif // ARM_COMPUTE_ENABLE_SVE2 + +/** Calculate n power of a number. + * + * pow(x,n) = e^(n*log(x)) + * + * @param[in] pg Input predicate. + * @param[in] a Input vector value in F32 format. + * @param[in] b Powers to raise the input to. + * + * @return The calculated power. + */ +svfloat32_t svpow_f32_z(svbool_t pg, svfloat32_t a, svfloat32_t b); + +/** Calculate n power of a number. + * + * pow(x,n) = e^(n*log(x)) + * + * @param[in] pg Input predicate. + * @param[in] a Input vector value in F16 format. + * @param[in] b Powers to raise the input to. + * + * @return The calculated power. + */ +svfloat16_t svpow_f16_z(svbool_t pg, svfloat16_t a, svfloat16_t b); + +#ifdef ARM_COMPUTE_ENABLE_SVE2 + +/** Calculate n power of a number. + * + * pow(x,n) = e^(n*log(x)) + * + * @param[in] pg Input predicate. + * @param[in] a Input vector value in F16 format. + * @param[in] b Powers to raise the input to. + * + * @return The calculated power. + */ +svfloat16_t svpow_f16_z_sve2(svbool_t pg, svfloat16_t a, svfloat16_t b); + +#endif // ARM_COMPUTE_ENABLE_SVE2 + +/** Convert and pack four 32-bit float vectors into an 8-bit integer vector + * + * @param[in] in_0 The first float vector + * @param[in] in_1 The second float vector + * @param[in] in_2 The third float vector + * @param[in] in_3 The fourth float vector + * + * @return The converted integer vector + */ +template <typename int_vec_type> +int_vec_type convert_float_to_int(const svfloat32_t &in_0, + const svfloat32_t &in_1, + const svfloat32_t &in_2, + const svfloat32_t &in_3); + +} // namespace arm_compute +#include "src/core/NEON/SVEMath.inl" +#endif /* defined(ARM_COMPUTE_ENABLE_SVE) */ +#endif // ACL_SRC_CORE_NEON_SVEMATH_H |