/* * 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(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 #include 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 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 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(ENABLE_SVE) */ #endif /* ARM_COMPUTE_SVEMATH_H */