| Index: webrtc/modules/audio_processing/aec3/vector_math.h
|
| diff --git a/webrtc/modules/audio_processing/aec3/vector_math.h b/webrtc/modules/audio_processing/aec3/vector_math.h
|
| index b943f2beddf91989544409338daaeb2cb61ddbc1..afd4262b6ba07ee6d58389ad7e991176360ba167 100644
|
| --- a/webrtc/modules/audio_processing/aec3/vector_math.h
|
| +++ b/webrtc/modules/audio_processing/aec3/vector_math.h
|
| @@ -12,9 +12,6 @@
|
| #define WEBRTC_MODULES_AUDIO_PROCESSING_AEC3_VECTOR_MATH_H_
|
|
|
| #include "webrtc/typedefs.h"
|
| -#if defined(WEBRTC_HAS_NEON)
|
| -#include <arm_neon.h>
|
| -#endif
|
| #if defined(WEBRTC_ARCH_X86_FAMILY)
|
| #include <emmintrin.h>
|
| #endif
|
| @@ -56,51 +53,6 @@
|
| }
|
| } break;
|
| #endif
|
| -#if defined(WEBRTC_HAS_NEON)
|
| - case Aec3Optimization::kNeon: {
|
| - const int x_size = static_cast<int>(x.size());
|
| - const int vector_limit = x_size >> 2;
|
| -
|
| - int j = 0;
|
| - for (; j < vector_limit * 4; j += 4) {
|
| - float32x4_t g = vld1q_f32(&x[j]);
|
| -#if !defined(WEBRTC_ARCH_ARM64)
|
| - float32x4_t y = vrsqrteq_f32(g);
|
| -
|
| - // Code to handle sqrt(0).
|
| - // If the input to sqrtf() is zero, a zero will be returned.
|
| - // If the input to vrsqrteq_f32() is zero, positive infinity is
|
| - // returned.
|
| - const uint32x4_t vec_p_inf = vdupq_n_u32(0x7F800000);
|
| - // check for divide by zero
|
| - const uint32x4_t div_by_zero =
|
| - vceqq_u32(vec_p_inf, vreinterpretq_u32_f32(y));
|
| - // zero out the positive infinity results
|
| - y = vreinterpretq_f32_u32(
|
| - vandq_u32(vmvnq_u32(div_by_zero), vreinterpretq_u32_f32(y)));
|
| - // from arm documentation
|
| - // The Newton-Raphson iteration:
|
| - // y[n+1] = y[n] * (3 - d * (y[n] * y[n])) / 2)
|
| - // converges to (1/√d) if y0 is the result of VRSQRTE applied to d.
|
| - //
|
| - // Note: The precision did not improve after 2 iterations.
|
| - for (int i = 0; i < 2; i++) {
|
| - y = vmulq_f32(vrsqrtsq_f32(vmulq_f32(y, y), g), y);
|
| - }
|
| - // sqrt(g) = g * 1/sqrt(g)
|
| - g = vmulq_f32(g, y);
|
| -#else
|
| - g = vsqrtq_f32(g);
|
| -#endif
|
| - vst1q_f32(&x[j], g);
|
| - }
|
| -
|
| - for (; j < x_size; ++j) {
|
| - x[j] = sqrtf(x[j]);
|
| - }
|
| - }
|
| -#endif
|
| - break;
|
| default:
|
| std::for_each(x.begin(), x.end(), [](float& a) { a = sqrtf(a); });
|
| }
|
| @@ -124,24 +76,6 @@
|
| const __m128 y_j = _mm_loadu_ps(&y[j]);
|
| const __m128 z_j = _mm_mul_ps(x_j, y_j);
|
| _mm_storeu_ps(&z[j], z_j);
|
| - }
|
| -
|
| - for (; j < x_size; ++j) {
|
| - z[j] = x[j] * y[j];
|
| - }
|
| - } break;
|
| -#endif
|
| -#if defined(WEBRTC_HAS_NEON)
|
| - case Aec3Optimization::kNeon: {
|
| - const int x_size = static_cast<int>(x.size());
|
| - const int vector_limit = x_size >> 2;
|
| -
|
| - int j = 0;
|
| - for (; j < vector_limit * 4; j += 4) {
|
| - const float32x4_t x_j = vld1q_f32(&x[j]);
|
| - const float32x4_t y_j = vld1q_f32(&y[j]);
|
| - const float32x4_t z_j = vmulq_f32(x_j, y_j);
|
| - vst1q_f32(&z[j], z_j);
|
| }
|
|
|
| for (; j < x_size; ++j) {
|
| @@ -177,24 +111,6 @@
|
| }
|
| } break;
|
| #endif
|
| -#if defined(WEBRTC_HAS_NEON)
|
| - case Aec3Optimization::kNeon: {
|
| - const int x_size = static_cast<int>(x.size());
|
| - const int vector_limit = x_size >> 2;
|
| -
|
| - int j = 0;
|
| - for (; j < vector_limit * 4; j += 4) {
|
| - const float32x4_t x_j = vld1q_f32(&x[j]);
|
| - float32x4_t z_j = vld1q_f32(&z[j]);
|
| - z_j = vaddq_f32(z_j, x_j);
|
| - vst1q_f32(&z[j], z_j);
|
| - }
|
| -
|
| - for (; j < x_size; ++j) {
|
| - z[j] += x[j];
|
| - }
|
| - } break;
|
| -#endif
|
| default:
|
| std::transform(x.begin(), x.end(), z.begin(), z.begin(),
|
| std::plus<float>());
|
|
|