ARM Skia NEON patches - 35 - First AArch64 support

src/core/SkBlitter_RGB16.cpp

 
 /*
  * Copyright 2006 The Android Open Source Project
  *
  * Use of this source code is governed by a BSD-style license that can be
  * found in the LICENSE file.
  */
 
 
 #include "SkBlitRow.h"
 #include "SkCoreBlitters.h"
 #include "SkColorPriv.h"
 #include "SkDither.h"
 #include "SkShader.h"
 #include "SkTemplatesPriv.h"
 #include "SkUtils.h"
 #include "SkXfermode.h"
 
-#if defined(__ARM_HAVE_NEON) && defined(SK_CPU_LENDIAN)
-    #define SK_USE_NEON
+#if SK_ARM_NEON_IS_ALWAYS && defined(SK_CPU_LENDIAN)

[djsollen, 2014/03/20 14:40:16]

can we do this in a separate CL since it doesn't seem to be tied to 64-bit? If
you want I'll be happy to take care of that.

[kevin.petit, 2014/03/20 16:05:09]

You're right. I've uploaded https://codereview.chromium.org/206543002/.

     #include <arm_neon.h>
 #else
     // if we don't have neon, then our black blitter is worth the extra code
     #define USE_BLACK_BLITTER
 #endif
 
 void sk_dither_memset16(uint16_t dst[], uint16_t value, uint16_t other,
                         int count) {
     if (count > 0) {
         // see if we need to write one short before we can cast to an 4byte ptr
@@ skipping 347 matching lines @@
     }
 
     uint16_t* SK_RESTRICT device = fDevice.getAddr16(clip.fLeft, clip.fTop);
     const uint8_t* SK_RESTRICT alpha = mask.getAddr8(clip.fLeft, clip.fTop);
     int width = clip.width();
     int height = clip.height();
     size_t      deviceRB = fDevice.rowBytes() - (width << 1);
     unsigned    maskRB = mask.fRowBytes - width;
     uint32_t    expanded32 = fExpandedRaw16;
 
-#ifdef SK_USE_NEON
+#if SK_ARM_NEON_IS_ALWAYS && defined(SK_CPU_LENDIAN)
 #define    UNROLL    8
     do {
         int w = width;
         if (w >= UNROLL) {
             uint32x4_t color, dev_lo, dev_hi;
             uint32x4_t wn1, wn2, tmp;
             uint32x4_t vmask_g16, vmask_ng16;
             uint16x8_t valpha, vdev;
             uint16x4_t odev_lo, odev_hi, valpha_lo, valpha_hi;
 
@@ skipping 647 matching lines @@
             SK_PLACEMENT_NEW_ARGS(blitter, SkRGB16_Opaque_Blitter, storage,
                                   storageSize, (device, paint));
         } else {
             SK_PLACEMENT_NEW_ARGS(blitter, SkRGB16_Blitter, storage,
                                   storageSize, (device, paint));
         }
     }
 
     return blitter;
 }