commit f3086f0b30b966f3ead7d0029678d742a8d0cc27
author Mike Klein <mtklein@google.com> Tue Dec 04 15:14:28 2018 -0500
committer Skia Commit-Bot <skia-commit-bot@chromium.org> Tue Dec 04 21:18:33 2018 +0000
tree 3423ea68dbd796df56d4d8581785103519ccfb4d
parent 4eb02aac2ddd417e7aa061311f048f19bf389524

split up SkColor_opts_SSE2.h

Lots of dead code deleted, and the rest moved where it's used.

Change-Id: I78804ce8563685b0b6aea7e8eb8a6656771d73fe
Reviewed-on: https://skia-review.googlesource.com/c/174286
Reviewed-by: Mike Klein <mtklein@google.com>
Commit-Queue: Mike Klein <mtklein@google.com>

src/opts/SkBlitRow_opts.h

diff --git a/src/opts/SkBlitRow_opts.h b/src/opts/SkBlitRow_opts.h
index 1b9ad30..a64730d 100644
--- a/src/opts/SkBlitRow_opts.h
+++ b/src/opts/SkBlitRow_opts.h
@@ -12,8 +12,30 @@
 #include "SkMSAN.h"
 
 #if SK_CPU_SSE_LEVEL >= SK_CPU_SSE_LEVEL_SSE2
-    #include "SkColor_opts_SSE2.h"
     #include <immintrin.h>
+
+    static inline __m128i SkPMSrcOver_SSE2(const __m128i& src, const __m128i& dst) {
+        auto SkAlphaMulQ_SSE2 = [](const __m128i& c, const __m128i& scale) {
+            const __m128i mask = _mm_set1_epi32(0xFF00FF);
+            __m128i s = _mm_or_si128(_mm_slli_epi32(scale, 16), scale);
+
+            // uint32_t rb = ((c & mask) * scale) >> 8
+            __m128i rb = _mm_and_si128(mask, c);
+            rb = _mm_mullo_epi16(rb, s);
+            rb = _mm_srli_epi16(rb, 8);
+
+            // uint32_t ag = ((c >> 8) & mask) * scale
+            __m128i ag = _mm_srli_epi16(c, 8);
+            ag = _mm_mullo_epi16(ag, s);
+
+            // (rb & mask) | (ag & ~mask)
+            ag = _mm_andnot_si128(mask, ag);
+            return _mm_or_si128(rb, ag);
+        };
+        return _mm_add_epi32(src,
+                             SkAlphaMulQ_SSE2(dst, _mm_sub_epi32(_mm_set1_epi32(256),
+                                                                 _mm_srli_epi32(src, 24))));
+    }
 #endif
 
 namespace SK_OPTS_NS {