diff options
author | Sang-Hoon Park <sang-hoon.park@arm.com> | 2020-12-08 18:42:19 +0000 |
---|---|---|
committer | Sang-Hoon Park <sang-hoon.park@arm.com> | 2021-01-04 13:53:41 +0000 |
commit | 0870db478fc46213138bcfd6e1536610ea145ecf (patch) | |
tree | 766cf948f9125d319248baee8101118c965d4de4 /src/core/NEON/SVEMath.h | |
parent | 8a8f4fac9776b036aec2a50b1473c30750ed32d2 (diff) | |
download | ComputeLibrary-0870db478fc46213138bcfd6e1536610ea145ecf.tar.gz |
Add utility functions for SVE
- Few bit-width dependent intrinsics are added.
- Few math functions are added.
Partially implements: COMPMID-3872
Change-Id: Ia6ab46bd170fec9c7c8d4410b7ef4d84710b68ed
Signed-off-by: Sang-Hoon Park <sang-hoon.park@arm.com>
Reviewed-on: https://review.mlplatform.org/c/ml/ComputeLibrary/+/4718
Tested-by: Arm Jenkins <bsgcomp@arm.com>
Reviewed-by: Michalis Spyrou <michalis.spyrou@arm.com>
Comments-Addressed: Arm Jenkins <bsgcomp@arm.com>
Diffstat (limited to 'src/core/NEON/SVEMath.h')
-rw-r--r-- | src/core/NEON/SVEMath.h | 62 |
1 files changed, 62 insertions, 0 deletions
diff --git a/src/core/NEON/SVEMath.h b/src/core/NEON/SVEMath.h index bdf2e894e2..490759c789 100644 --- a/src/core/NEON/SVEMath.h +++ b/src/core/NEON/SVEMath.h @@ -25,6 +25,10 @@ #define ARM_COMPUTE_SVEMATH_H #if defined(__ARM_FEATURE_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 "src/core/common/StdTypes.h" #include <arm_sve.h> #include <array> @@ -110,6 +114,64 @@ svfloat16_t svinv_f16_z(svbool_t pg, svfloat16_t x); */ svfloat16_t svlog_f16_z(svbool_t pg, svfloat16_t x); +/** Calculate inverse square root. + * + * @param[in] pg Input reciprocal. + * @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 reciprocal. + * @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 reciprocal. + * @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 reciprocal. + * @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 reciprocal. + * @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); + } // namespace arm_compute #include "src/core/NEON/SVEMath.inl" #endif /* defined(__ARM_FEATURE_SVE) */ |