ARM Skia NEON patches - 31 - Xfermode: xfer16

src/opts/SkColor_opts_neon.h

 #ifndef SkColor_opts_neon_DEFINED
 #define SkColor_opts_neon_DEFINED
 
 #include "SkTypes.h"
 
 #include <arm_neon.h>
 
 #define NEON_A (SK_A32_SHIFT / 8)
 #define NEON_R (SK_R32_SHIFT / 8)
 #define NEON_G (SK_G32_SHIFT / 8)
@@ skipping 11 matching lines @@
     uint8x8x4_t ret;
 
     ret.val[NEON_A] = SkAlphaMul_neon8(color.val[NEON_A], scale);
     ret.val[NEON_R] = SkAlphaMul_neon8(color.val[NEON_R], scale);
     ret.val[NEON_G] = SkAlphaMul_neon8(color.val[NEON_G], scale);
     ret.val[NEON_B] = SkAlphaMul_neon8(color.val[NEON_B], scale);
 
     return ret;
 }
 
+/* This function expands 8 pixels from RGB565 (R, G, B from high to low) to
+ * SkPMColor (all possible configurations supported) in the exact same way as
+ * SkPixel16ToPixel32.
+ */
+static inline uint8x8x4_t SkPixel16ToPixel32_neon8(uint16x8_t vsrc) {
+
+    uint8x8x4_t ret;
+    uint8x8_t vr, vg, vb;
+
+    vr = vmovn_u16(vshrq_n_u16(vsrc, SK_R16_SHIFT));
+    vg = vmovn_u16(vshrq_n_u16(vshlq_n_u16(vsrc, SK_R16_BITS), SK_R16_BITS + SK_B16_BITS));
+    vb = vmovn_u16(vsrc & vdupq_n_u16(SK_B16_MASK));
+
+    ret.val[NEON_A] = vdup_n_u8(0xFF);
+    ret.val[NEON_R] = vshl_n_u8(vr, 8 - SK_R16_BITS) | vshr_n_u8(vr, 2 * SK_R16_BITS - 8);
+    ret.val[NEON_G] = vshl_n_u8(vg, 8 - SK_G16_BITS) | vshr_n_u8(vg, 2 * SK_G16_BITS - 8);
+    ret.val[NEON_B] = vshl_n_u8(vb, 8 - SK_B16_BITS) | vshr_n_u8(vb, 2 * SK_B16_BITS - 8);
+
+    return ret;
+}
+
+/* This function packs 8 pixels from SkPMColor (all possible configurations
+ * supported) to RGB565 (R, G, B from high to low) in the exact same way as
+ * SkPixel32ToPixel16.
+ */
+static inline uint16x8_t SkPixel32ToPixel16_neon8(uint8x8x4_t vsrc) {
+
+    uint16x8_t ret;
+
+    ret = vshll_n_u8(vsrc.val[NEON_R], 8);
+    ret = vsriq_n_u16(ret, vshll_n_u8(vsrc.val[NEON_G], 8), SK_R16_BITS);
+    ret = vsriq_n_u16(ret, vshll_n_u8(vsrc.val[NEON_B], 8), SK_R16_BITS + SK_G16_BITS);
+
+    return ret;
+}
+
 #endif /* #ifndef SkColor_opts_neon_DEFINED */