diff options
author | Eric Laurent <elaurent@google.com> | 2012-01-31 14:20:52 -0800 |
---|---|---|
committer | Eric Laurent <elaurent@google.com> | 2012-02-02 08:57:35 -0800 |
commit | c55a96383497a772a307b346368133960b02ad03 (patch) | |
tree | 43b7aaa9cf8b8d42d0d58e123d27e37ad96607a5 /src/common_audio/signal_processing/min_max_operations_neon.c | |
parent | 4b6dc1ec58105d17dc8c2f550124cc0621dc93b7 (diff) | |
download | webrtc-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.c | 47 |
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 |