OLD | NEW |
1 /* | 1 /* |
2 * Copyright (C) 2010, Google Inc. All rights reserved. | 2 * Copyright (C) 2010, Google Inc. All rights reserved. |
3 * | 3 * |
4 * Redistribution and use in source and binary forms, with or without | 4 * Redistribution and use in source and binary forms, with or without |
5 * modification, are permitted provided that the following conditions | 5 * modification, are permitted provided that the following conditions |
6 * are met: | 6 * are met: |
7 * 1. Redistributions of source code must retain the above copyright | 7 * 1. Redistributions of source code must retain the above copyright |
8 * notice, this list of conditions and the following disclaimer. | 8 * notice, this list of conditions and the following disclaimer. |
9 * 2. Redistributions in binary form must reproduce the above copyright | 9 * 2. Redistributions in binary form must reproduce the above copyright |
10 * notice, this list of conditions and the following disclaimer in the | 10 * notice, this list of conditions and the following disclaimer in the |
(...skipping 10 matching lines...) Expand all Loading... |
21 * (INCLUDING NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS | 21 * (INCLUDING NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS |
22 * SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. | 22 * SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. |
23 */ | 23 */ |
24 | 24 |
25 #include "config.h" | 25 #include "config.h" |
26 | 26 |
27 #if ENABLE(WEB_AUDIO) | 27 #if ENABLE(WEB_AUDIO) |
28 | 28 |
29 #include "core/platform/audio/VectorMath.h" | 29 #include "core/platform/audio/VectorMath.h" |
30 #include "wtf/Assertions.h" | 30 #include "wtf/Assertions.h" |
| 31 #include "wtf/CPU.h" |
31 #include <stdint.h> | 32 #include <stdint.h> |
32 | 33 |
33 #if OS(MACOSX) | 34 #if OS(MACOSX) |
34 #include <Accelerate/Accelerate.h> | 35 #include <Accelerate/Accelerate.h> |
35 #endif | 36 #endif |
36 | 37 |
37 #ifdef __SSE2__ | 38 #ifdef __SSE2__ |
38 #include <emmintrin.h> | 39 #include <emmintrin.h> |
39 #endif | 40 #endif |
40 | 41 |
41 #if HAVE(ARM_NEON_INTRINSICS) | 42 #if HAVE(ARM_NEON_INTRINSICS) |
42 #include <arm_neon.h> | 43 #include <arm_neon.h> |
43 #endif | 44 #endif |
44 | 45 |
45 #include <math.h> | 46 #include <math.h> |
46 #include <algorithm> | 47 #include <algorithm> |
47 | 48 |
48 namespace WebCore { | 49 namespace WebCore { |
49 | 50 |
50 namespace VectorMath { | 51 namespace VectorMath { |
51 | 52 |
52 #if OS(MACOSX) | 53 #if OS(MACOSX) |
53 // On the Mac we use the highly optimized versions in Accelerate.framework | 54 // On the Mac we use the highly optimized versions in Accelerate.framework |
54 // In 32-bit mode (__ppc__ or __i386__) <Accelerate/Accelerate.h> includes <vecL
ib/vDSP_translate.h> which defines macros of the same name as | 55 // In 32-bit mode (__ppc__ or __i386__) <Accelerate/Accelerate.h> includes <vecL
ib/vDSP_translate.h> which defines macros of the same name as |
55 // our namespaced function names, so we must handle this case differently. Other
architectures (64bit, ARM, etc.) do not include this header file. | 56 // our namespaced function names, so we must handle this case differently. Other
architectures (64bit, ARM, etc.) do not include this header file. |
56 | 57 |
57 void vsmul(const float* sourceP, int sourceStride, const float* scale, float* de
stP, int destStride, size_t framesToProcess) | 58 void vsmul(const float* sourceP, int sourceStride, const float* scale, float* de
stP, int destStride, size_t framesToProcess) |
58 { | 59 { |
59 #if defined(__i386__) | 60 #if CPU(X86) |
60 ::vsmul(sourceP, sourceStride, scale, destP, destStride, framesToProcess); | 61 ::vsmul(sourceP, sourceStride, scale, destP, destStride, framesToProcess); |
61 #else | 62 #else |
62 vDSP_vsmul(sourceP, sourceStride, scale, destP, destStride, framesToProcess)
; | 63 vDSP_vsmul(sourceP, sourceStride, scale, destP, destStride, framesToProcess)
; |
63 #endif | 64 #endif |
64 } | 65 } |
65 | 66 |
66 void vadd(const float* source1P, int sourceStride1, const float* source2P, int s
ourceStride2, float* destP, int destStride, size_t framesToProcess) | 67 void vadd(const float* source1P, int sourceStride1, const float* source2P, int s
ourceStride2, float* destP, int destStride, size_t framesToProcess) |
67 { | 68 { |
68 #if defined(__i386__) | 69 #if CPU(X86) |
69 ::vadd(source1P, sourceStride1, source2P, sourceStride2, destP, destStride,
framesToProcess); | 70 ::vadd(source1P, sourceStride1, source2P, sourceStride2, destP, destStride,
framesToProcess); |
70 #else | 71 #else |
71 vDSP_vadd(source1P, sourceStride1, source2P, sourceStride2, destP, destStrid
e, framesToProcess); | 72 vDSP_vadd(source1P, sourceStride1, source2P, sourceStride2, destP, destStrid
e, framesToProcess); |
72 #endif | 73 #endif |
73 } | 74 } |
74 | 75 |
75 void vmul(const float* source1P, int sourceStride1, const float* source2P, int s
ourceStride2, float* destP, int destStride, size_t framesToProcess) | 76 void vmul(const float* source1P, int sourceStride1, const float* source2P, int s
ourceStride2, float* destP, int destStride, size_t framesToProcess) |
76 { | 77 { |
77 #if defined(__i386__) | 78 #if CPU(X86) |
78 ::vmul(source1P, sourceStride1, source2P, sourceStride2, destP, destStride,
framesToProcess); | 79 ::vmul(source1P, sourceStride1, source2P, sourceStride2, destP, destStride,
framesToProcess); |
79 #else | 80 #else |
80 vDSP_vmul(source1P, sourceStride1, source2P, sourceStride2, destP, destStrid
e, framesToProcess); | 81 vDSP_vmul(source1P, sourceStride1, source2P, sourceStride2, destP, destStrid
e, framesToProcess); |
81 #endif | 82 #endif |
82 } | 83 } |
83 | 84 |
84 void zvmul(const float* real1P, const float* imag1P, const float* real2P, const
float* imag2P, float* realDestP, float* imagDestP, size_t framesToProcess) | 85 void zvmul(const float* real1P, const float* imag1P, const float* real2P, const
float* imag2P, float* realDestP, float* imagDestP, size_t framesToProcess) |
85 { | 86 { |
86 DSPSplitComplex sc1; | 87 DSPSplitComplex sc1; |
87 DSPSplitComplex sc2; | 88 DSPSplitComplex sc2; |
88 DSPSplitComplex dest; | 89 DSPSplitComplex dest; |
89 sc1.realp = const_cast<float*>(real1P); | 90 sc1.realp = const_cast<float*>(real1P); |
90 sc1.imagp = const_cast<float*>(imag1P); | 91 sc1.imagp = const_cast<float*>(imag1P); |
91 sc2.realp = const_cast<float*>(real2P); | 92 sc2.realp = const_cast<float*>(real2P); |
92 sc2.imagp = const_cast<float*>(imag2P); | 93 sc2.imagp = const_cast<float*>(imag2P); |
93 dest.realp = realDestP; | 94 dest.realp = realDestP; |
94 dest.imagp = imagDestP; | 95 dest.imagp = imagDestP; |
95 #if defined(__i386__) | 96 #if CPU(X86) |
96 ::zvmul(&sc1, 1, &sc2, 1, &dest, 1, framesToProcess, 1); | 97 ::zvmul(&sc1, 1, &sc2, 1, &dest, 1, framesToProcess, 1); |
97 #else | 98 #else |
98 vDSP_zvmul(&sc1, 1, &sc2, 1, &dest, 1, framesToProcess, 1); | 99 vDSP_zvmul(&sc1, 1, &sc2, 1, &dest, 1, framesToProcess, 1); |
99 #endif | 100 #endif |
100 } | 101 } |
101 | 102 |
102 void vsma(const float* sourceP, int sourceStride, const float* scale, float* des
tP, int destStride, size_t framesToProcess) | 103 void vsma(const float* sourceP, int sourceStride, const float* scale, float* des
tP, int destStride, size_t framesToProcess) |
103 { | 104 { |
104 vDSP_vsma(sourceP, sourceStride, scale, destP, destStride, destP, destStride
, framesToProcess); | 105 vDSP_vsma(sourceP, sourceStride, scale, destP, destStride, destP, destStride
, framesToProcess); |
105 } | 106 } |
(...skipping 574 matching lines...) Expand 10 before | Expand all | Expand 10 after Loading... |
680 } | 681 } |
681 } | 682 } |
682 | 683 |
683 #endif // OS(MACOSX) | 684 #endif // OS(MACOSX) |
684 | 685 |
685 } // namespace VectorMath | 686 } // namespace VectorMath |
686 | 687 |
687 } // namespace WebCore | 688 } // namespace WebCore |
688 | 689 |
689 #endif // ENABLE(WEB_AUDIO) | 690 #endif // ENABLE(WEB_AUDIO) |
OLD | NEW |