aboutsummaryrefslogtreecommitdiff
path: root/src/common_audio/signal_processing/min_max_operations_neon.c
diff options
context:
space:
mode:
authorEric Laurent <elaurent@google.com>2012-01-31 14:20:52 -0800
committerEric Laurent <elaurent@google.com>2012-02-02 08:57:35 -0800
commitc55a96383497a772a307b346368133960b02ad03 (patch)
tree43b7aaa9cf8b8d42d0d58e123d27e37ad96607a5 /src/common_audio/signal_processing/min_max_operations_neon.c
parent4b6dc1ec58105d17dc8c2f550124cc0621dc93b7 (diff)
downloadwebrtc-c55a96383497a772a307b346368133960b02ad03.tar.gz
update to webrtc revision 1349
Updated audio processing modules from revision 180 to 1349. Main changes are: - code clean up and reformating - source path reorganization - improved performance Also imported test code that was not included in initial drop from webrtc. Change-Id: Ie4eb0e29990052e5f2d7f0b271b42eead40dbb6a
Diffstat (limited to 'src/common_audio/signal_processing/min_max_operations_neon.c')
-rw-r--r--src/common_audio/signal_processing/min_max_operations_neon.c47
1 files changed, 47 insertions, 0 deletions
diff --git a/src/common_audio/signal_processing/min_max_operations_neon.c b/src/common_audio/signal_processing/min_max_operations_neon.c
new file mode 100644
index 0000000000..158bcc1837
--- /dev/null
+++ b/src/common_audio/signal_processing/min_max_operations_neon.c
@@ -0,0 +1,47 @@
+/*
+ * Copyright (c) 2011 The WebRTC project authors. All Rights Reserved.
+ *
+ * Use of this source code is governed by a BSD-style license
+ * that can be found in the LICENSE file in the root of the source
+ * tree. An additional intellectual property rights grant can be found
+ * in the file PATENTS. All contributing project authors may
+ * be found in the AUTHORS file in the root of the source tree.
+ */
+
+#if (defined(WEBRTC_ANDROID) && defined(WEBRTC_ARCH_ARM_NEON))
+
+#include <arm_neon.h>
+
+#include "signal_processing_library.h"
+
+// Maximum absolute value of word16 vector.
+WebRtc_Word16 WebRtcSpl_MaxAbsValueW16(const WebRtc_Word16* vector,
+ WebRtc_Word16 length) {
+ WebRtc_Word32 temp_max = 0;
+ WebRtc_Word32 abs_val;
+ WebRtc_Word16 tot_max;
+ int i;
+
+ __asm__("vmov.i16 d25, #0" : : : "d25");
+
+ for (i = 0; i < length - 7; i += 8) {
+ __asm__("vld1.16 {d26, d27}, [%0]" : : "r"(&vector[i]) : "q13");
+ __asm__("vabs.s16 q13, q13" : : : "q13");
+ __asm__("vpmax.s16 d26, d27" : : : "q13");
+ __asm__("vpmax.s16 d25, d26" : : : "d25", "d26");
+ }
+ __asm__("vpmax.s16 d25, d25" : : : "d25");
+ __asm__("vpmax.s16 d25, d25" : : : "d25");
+ __asm__("vmov.s16 %0, d25[0]" : "=r"(temp_max): : "d25");
+
+ for (; i < length; i++) {
+ abs_val = WEBRTC_SPL_ABS_W32((vector[i]));
+ if (abs_val > temp_max) {
+ temp_max = abs_val;
+ }
+ }
+ tot_max = (WebRtc_Word16)WEBRTC_SPL_MIN(temp_max, WEBRTC_SPL_WORD16_MAX);
+ return tot_max;
+}
+
+#endif