| /* |
| * Copyright (c) 2020-2021 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 ARM_COMPUTE_SVEMATH_H |
| #define ARM_COMPUTE_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); |
| |
| /** 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); |
| |
| /** 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); |
| |
| /** 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); |
| |
| /** 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 /* ARM_COMPUTE_SVEMATH_H */ |