Changeset 132890 in webkit

Timestamp:

Oct 30, 2012 3:50:42 AM (11 years ago)

Author:

rgabor@webkit.org

Message:

Optimize vclip for NEON in VectorMath
​https://bugs.webkit.org/show_bug.cgi?id=100737

Reviewed by Zoltan Herczeg.

Speed up vclip in VectorMath with NEON intrinsics.

• platform/audio/VectorMath.cpp:

(WebCore::VectorMath::vclip):

Location:

trunk/Source/WebCore

Files:

• ChangeLog (modified) (1 diff)
• platform/audio/VectorMath.cpp (modified) (1 diff)

trunk/Source/WebCore/ChangeLog

@@ +1 @@
+2012-10-30  Gabor Rapcsanyi  <rgabor@webkit.org>
+
+        Optimize vclip for NEON in VectorMath
+        https://bugs.webkit.org/show_bug.cgi?id=100737
+
+        Reviewed by Zoltan Herczeg.
+
+        Speed up vclip in VectorMath with NEON intrinsics.
+
+        * platform/audio/VectorMath.cpp:
+        (WebCore::VectorMath::vclip):
+
 2012-10-30  Alexandru Chiculita  <achicu@adobe.com>
 

trunk/Source/WebCore/platform/audio/VectorMath.cpp

@@ -656 +656 @@
 
     // FIXME: Optimize for SSE2.
-    // FIXME: Optimize for NEON.
+#if HAVE(ARM_NEON_INTRINSICS)
+    if ((sourceStride == 1) && (destStride == 1)) {
+        int tailFrames = n % 4;
+        const float* endP = destP + n - tailFrames;
+
+        float32x4_t low = vdupq_n_f32(lowThreshold);
+        float32x4_t high = vdupq_n_f32(highThreshold);
+        while (destP < endP) {
+            float32x4_t source = vld1q_f32(sourceP);
+            vst1q_f32(destP, vmaxq_f32(vminq_f32(source, high), low));
+            sourceP += 4;
+            destP += 4;
+        }
+        n = tailFrames;
+    }
+#endif
     while (n--) {
         *destP = std::max(std::min(*sourceP, highThreshold), lowThreshold);