2015-02-13 16:07:08 -08:00
|
|
|
// This file is part of Eigen, a lightweight C++ template library
|
|
|
|
|
// for linear algebra.
|
|
|
|
|
//
|
|
|
|
|
// Copyright (C) 2014 Pedro Gonnet (pedro.gonnet@gmail.com)
|
|
|
|
|
//
|
|
|
|
|
// This Source Code Form is subject to the terms of the Mozilla
|
|
|
|
|
// Public License v. 2.0. If a copy of the MPL was not distributed
|
|
|
|
|
// with this file, You can obtain one at http://mozilla.org/MPL/2.0/.
|
|
|
|
|
|
|
|
|
|
#ifndef EIGEN_MATH_FUNCTIONS_AVX_H
|
|
|
|
|
#define EIGEN_MATH_FUNCTIONS_AVX_H
|
|
|
|
|
|
2018-11-26 23:21:29 +01:00
|
|
|
/* The sin and cos functions of this file are loosely derived from
|
2015-02-13 16:07:08 -08:00
|
|
|
* Julien Pommier's sse math library: http://gruntthepeon.free.fr/ssemath/
|
|
|
|
|
*/
|
|
|
|
|
|
2023-08-21 16:25:22 +00:00
|
|
|
// IWYU pragma: private
|
2021-09-10 19:12:26 +00:00
|
|
|
#include "../../InternalHeaderCheck.h"
|
|
|
|
|
|
2015-02-13 16:07:08 -08:00
|
|
|
namespace Eigen {
|
|
|
|
|
|
|
|
|
|
namespace internal {
|
|
|
|
|
|
2023-03-10 22:02:23 +00:00
|
|
|
EIGEN_INSTANTIATE_GENERIC_MATH_FUNCS_FLOAT(Packet8f)
|
2024-04-16 16:12:41 +00:00
|
|
|
|
2024-08-30 17:27:55 +00:00
|
|
|
EIGEN_DOUBLE_PACKET_FUNCTION(atanh, Packet4d)
|
2024-04-17 16:55:45 +00:00
|
|
|
EIGEN_DOUBLE_PACKET_FUNCTION(log, Packet4d)
|
|
|
|
|
EIGEN_DOUBLE_PACKET_FUNCTION(log2, Packet4d)
|
|
|
|
|
EIGEN_DOUBLE_PACKET_FUNCTION(exp, Packet4d)
|
2024-08-21 02:29:45 +00:00
|
|
|
EIGEN_DOUBLE_PACKET_FUNCTION(tanh, Packet4d)
|
2025-04-17 23:31:20 +00:00
|
|
|
EIGEN_DOUBLE_PACKET_FUNCTION(cbrt, Packet4d)
|
2024-04-16 16:12:41 +00:00
|
|
|
#ifdef EIGEN_VECTORIZE_AVX2
|
2024-04-17 16:55:45 +00:00
|
|
|
EIGEN_DOUBLE_PACKET_FUNCTION(sin, Packet4d)
|
|
|
|
|
EIGEN_DOUBLE_PACKET_FUNCTION(cos, Packet4d)
|
2024-04-16 16:12:41 +00:00
|
|
|
#endif
|
2024-10-22 22:09:34 +00:00
|
|
|
EIGEN_GENERIC_PACKET_FUNCTION(atan, Packet4d)
|
|
|
|
|
EIGEN_GENERIC_PACKET_FUNCTION(exp2, Packet4d)
|
2024-08-21 20:44:18 +00:00
|
|
|
|
2022-02-23 17:32:21 +00:00
|
|
|
// Notice that for newer processors, it is counterproductive to use Newton
|
|
|
|
|
// iteration for square root. In particular, Skylake and Zen2 processors
|
|
|
|
|
// have approximately doubled throughput of the _mm_sqrt_ps instruction
|
|
|
|
|
// compared to their predecessors.
|
2022-03-03 20:19:33 +00:00
|
|
|
template <>
|
|
|
|
|
EIGEN_DEFINE_FUNCTION_ALLOWING_MULTIPLE_DEFINITIONS Packet8f psqrt<Packet8f>(const Packet8f& _x) {
|
2020-07-14 01:34:03 +00:00
|
|
|
return _mm256_sqrt_ps(_x);
|
2015-02-13 16:07:08 -08:00
|
|
|
}
|
2022-03-03 20:19:33 +00:00
|
|
|
template <>
|
|
|
|
|
EIGEN_DEFINE_FUNCTION_ALLOWING_MULTIPLE_DEFINITIONS Packet4d psqrt<Packet4d>(const Packet4d& _x) {
|
2020-07-14 01:34:03 +00:00
|
|
|
return _mm256_sqrt_pd(_x);
|
2015-02-13 16:07:08 -08:00
|
|
|
}
|
2015-03-02 09:38:47 -08:00
|
|
|
|
2022-02-23 17:32:21 +00:00
|
|
|
// Even on Skylake, using Newton iteration is a win for reciprocal square root.
|
2020-12-16 18:16:11 +00:00
|
|
|
#if EIGEN_FAST_MATH
|
2022-03-03 20:19:33 +00:00
|
|
|
template <>
|
|
|
|
|
EIGEN_DEFINE_FUNCTION_ALLOWING_MULTIPLE_DEFINITIONS Packet8f prsqrt<Packet8f>(const Packet8f& a) {
|
2022-03-02 17:20:47 +00:00
|
|
|
// _mm256_rsqrt_ps returns -inf for negative denormals.
|
|
|
|
|
// _mm512_rsqrt**_ps returns -NaN for negative denormals. We may want
|
|
|
|
|
// consistency here.
|
|
|
|
|
// const Packet8f rsqrt = pselect(pcmp_lt(a, pzero(a)),
|
|
|
|
|
// pset1<Packet8f>(-NumTraits<float>::quiet_NaN()),
|
|
|
|
|
// _mm256_rsqrt_ps(a));
|
2022-02-05 00:20:13 +00:00
|
|
|
return generic_rsqrt_newton_step<Packet8f, /*Steps=*/1>::run(a, _mm256_rsqrt_ps(a));
|
2015-03-02 09:38:47 -08:00
|
|
|
}
|
|
|
|
|
|
2022-01-21 23:49:18 +00:00
|
|
|
template <>
|
|
|
|
|
EIGEN_STRONG_INLINE Packet8f preciprocal<Packet8f>(const Packet8f& a) {
|
|
|
|
|
return generic_reciprocal_newton_step<Packet8f, /*Steps=*/1>::run(a, _mm256_rcp_ps(a));
|
2015-02-26 09:42:41 -08:00
|
|
|
}
|
2022-01-21 23:49:18 +00:00
|
|
|
|
2015-02-26 09:42:41 -08:00
|
|
|
#endif
|
2015-03-02 09:38:47 -08:00
|
|
|
|
2021-01-20 19:00:09 -08:00
|
|
|
template <>
|
|
|
|
|
EIGEN_STRONG_INLINE Packet8h pfrexp(const Packet8h& a, Packet8h& exponent) {
|
|
|
|
|
Packet8f fexponent;
|
|
|
|
|
const Packet8h out = float2half(pfrexp<Packet8f>(half2float(a), fexponent));
|
|
|
|
|
exponent = float2half(fexponent);
|
|
|
|
|
return out;
|
|
|
|
|
}
|
|
|
|
|
|
|
|
|
|
template <>
|
|
|
|
|
EIGEN_STRONG_INLINE Packet8h pldexp(const Packet8h& a, const Packet8h& exponent) {
|
|
|
|
|
return float2half(pldexp<Packet8f>(half2float(a), half2float(exponent)));
|
|
|
|
|
}
|
|
|
|
|
|
|
|
|
|
template <>
|
|
|
|
|
EIGEN_STRONG_INLINE Packet8bf pfrexp(const Packet8bf& a, Packet8bf& exponent) {
|
|
|
|
|
Packet8f fexponent;
|
|
|
|
|
const Packet8bf out = F32ToBf16(pfrexp<Packet8f>(Bf16ToF32(a), fexponent));
|
|
|
|
|
exponent = F32ToBf16(fexponent);
|
|
|
|
|
return out;
|
|
|
|
|
}
|
|
|
|
|
|
|
|
|
|
template <>
|
|
|
|
|
EIGEN_STRONG_INLINE Packet8bf pldexp(const Packet8bf& a, const Packet8bf& exponent) {
|
|
|
|
|
return F32ToBf16(pldexp<Packet8f>(Bf16ToF32(a), Bf16ToF32(exponent)));
|
|
|
|
|
}
|
|
|
|
|
|
2023-03-10 22:02:23 +00:00
|
|
|
BF16_PACKET_FUNCTION(Packet8f, Packet8bf, pcos)
|
|
|
|
|
BF16_PACKET_FUNCTION(Packet8f, Packet8bf, pexp)
|
2024-10-22 22:09:34 +00:00
|
|
|
BF16_PACKET_FUNCTION(Packet8f, Packet8bf, pexp2)
|
2023-03-10 22:02:23 +00:00
|
|
|
BF16_PACKET_FUNCTION(Packet8f, Packet8bf, pexpm1)
|
|
|
|
|
BF16_PACKET_FUNCTION(Packet8f, Packet8bf, plog)
|
|
|
|
|
BF16_PACKET_FUNCTION(Packet8f, Packet8bf, plog1p)
|
|
|
|
|
BF16_PACKET_FUNCTION(Packet8f, Packet8bf, plog2)
|
|
|
|
|
BF16_PACKET_FUNCTION(Packet8f, Packet8bf, preciprocal)
|
|
|
|
|
BF16_PACKET_FUNCTION(Packet8f, Packet8bf, prsqrt)
|
|
|
|
|
BF16_PACKET_FUNCTION(Packet8f, Packet8bf, psin)
|
|
|
|
|
BF16_PACKET_FUNCTION(Packet8f, Packet8bf, psqrt)
|
|
|
|
|
BF16_PACKET_FUNCTION(Packet8f, Packet8bf, ptanh)
|
2025-03-19 19:55:26 +00:00
|
|
|
|
|
|
|
|
#ifndef EIGEN_VECTORIZE_AVX512FP16
|
2023-03-10 22:02:23 +00:00
|
|
|
F16_PACKET_FUNCTION(Packet8f, Packet8h, pcos)
|
|
|
|
|
F16_PACKET_FUNCTION(Packet8f, Packet8h, pexp)
|
2024-10-22 22:09:34 +00:00
|
|
|
F16_PACKET_FUNCTION(Packet8f, Packet8h, pexp2)
|
2023-03-10 22:02:23 +00:00
|
|
|
F16_PACKET_FUNCTION(Packet8f, Packet8h, pexpm1)
|
|
|
|
|
F16_PACKET_FUNCTION(Packet8f, Packet8h, plog)
|
|
|
|
|
F16_PACKET_FUNCTION(Packet8f, Packet8h, plog1p)
|
|
|
|
|
F16_PACKET_FUNCTION(Packet8f, Packet8h, plog2)
|
|
|
|
|
F16_PACKET_FUNCTION(Packet8f, Packet8h, preciprocal)
|
|
|
|
|
F16_PACKET_FUNCTION(Packet8f, Packet8h, prsqrt)
|
|
|
|
|
F16_PACKET_FUNCTION(Packet8f, Packet8h, psin)
|
|
|
|
|
F16_PACKET_FUNCTION(Packet8f, Packet8h, psqrt)
|
|
|
|
|
F16_PACKET_FUNCTION(Packet8f, Packet8h, ptanh)
|
2025-03-19 19:55:26 +00:00
|
|
|
#endif
|
2023-03-10 22:02:23 +00:00
|
|
|
|
2015-02-13 16:07:08 -08:00
|
|
|
} // end namespace internal
|
|
|
|
|
|
|
|
|
|
} // end namespace Eigen
|
|
|
|
|
|
|
|
|
|
#endif // EIGEN_MATH_FUNCTIONS_AVX_H
|