1ec3ed6a5ebf6f2c406d7bcf94b6bc34fcaeb976eepoger@google.com 2ec3ed6a5ebf6f2c406d7bcf94b6bc34fcaeb976eepoger@google.com/* 3ec3ed6a5ebf6f2c406d7bcf94b6bc34fcaeb976eepoger@google.com * Copyright 2006 The Android Open Source Project 4ec3ed6a5ebf6f2c406d7bcf94b6bc34fcaeb976eepoger@google.com * 5ec3ed6a5ebf6f2c406d7bcf94b6bc34fcaeb976eepoger@google.com * Use of this source code is governed by a BSD-style license that can be 6ec3ed6a5ebf6f2c406d7bcf94b6bc34fcaeb976eepoger@google.com * found in the LICENSE file. 7ec3ed6a5ebf6f2c406d7bcf94b6bc34fcaeb976eepoger@google.com */ 8ec3ed6a5ebf6f2c406d7bcf94b6bc34fcaeb976eepoger@google.com 98a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 108a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#include "SkBlitRow.h" 118a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#include "SkCoreBlitters.h" 128a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#include "SkColorPriv.h" 138a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#include "SkDither.h" 148a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#include "SkShader.h" 158a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#include "SkUtils.h" 16e552dc82be1512df0a8a7f24310d27d2740d7601djsollen@google.com#include "SkUtilsArm.h" 178a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#include "SkXfermode.h" 188a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 1989351ec35a05eaf59edb7431d23a754cd084a363commit-bot@chromium.org#if SK_ARM_NEON_IS_ALWAYS && defined(SK_CPU_LENDIAN) 20867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com #include <arm_neon.h> 21867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com#else 22867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com // if we don't have neon, then our black blitter is worth the extra code 23867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com #define USE_BLACK_BLITTER 24867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com#endif 25867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com 268a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comvoid sk_dither_memset16(uint16_t dst[], uint16_t value, uint16_t other, 278a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int count) { 288a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (count > 0) { 298a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com // see if we need to write one short before we can cast to an 4byte ptr 308a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com // (we do this subtract rather than (unsigned)dst so we don't get warnings 318a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com // on 64bit machines) 328a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (((char*)dst - (char*)0) & 2) { 338a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com *dst++ = value; 348a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com count -= 1; 358a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkTSwap(value, other); 368a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 37fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 388a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com // fast way to set [value,other] pairs 398a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#ifdef SK_CPU_BENDIAN 408a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com sk_memset32((uint32_t*)dst, (value << 16) | other, count >> 1); 418a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#else 428a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com sk_memset32((uint32_t*)dst, (other << 16) | value, count >> 1); 438a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#endif 44fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 458a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (count & 1) { 468a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com dst[count - 1] = value; 478a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 488a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 498a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 508a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 518a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com/////////////////////////////////////////////////////////////////////////////// 528a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 531fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.comclass SkRGB16_Blitter : public SkRasterBlitter { 541fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.compublic: 551fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkRGB16_Blitter(const SkBitmap& device, const SkPaint& paint); 561fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com virtual void blitH(int x, int y, int width); 57a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com virtual void blitAntiH(int x, int y, const SkAlpha* antialias, 58a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com const int16_t* runs); 591fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com virtual void blitV(int x, int y, int height, SkAlpha alpha); 601fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com virtual void blitRect(int x, int y, int width, int height); 61a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com virtual void blitMask(const SkMask&, 62a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com const SkIRect&); 631fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com virtual const SkBitmap* justAnOpaqueColor(uint32_t*); 64fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 651fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.comprotected: 661fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkPMColor fSrcColor32; 67ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com uint32_t fExpandedRaw16; 681fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com unsigned fScale; 691fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com uint16_t fColor16; // already scaled by fScale 701fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com uint16_t fRawColor16; // unscaled 711fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com uint16_t fRawDither16; // unscaled 721fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkBool8 fDoDither; 73fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 741fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com // illegal 751fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkRGB16_Blitter& operator=(const SkRGB16_Blitter&); 76fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 771fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com typedef SkRasterBlitter INHERITED; 781fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com}; 791fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com 801fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.comclass SkRGB16_Opaque_Blitter : public SkRGB16_Blitter { 811fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.compublic: 821fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkRGB16_Opaque_Blitter(const SkBitmap& device, const SkPaint& paint); 831fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com virtual void blitH(int x, int y, int width); 84a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com virtual void blitAntiH(int x, int y, const SkAlpha* antialias, 85a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com const int16_t* runs); 86ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com virtual void blitV(int x, int y, int height, SkAlpha alpha); 871fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com virtual void blitRect(int x, int y, int width, int height); 88a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com virtual void blitMask(const SkMask&, 89a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com const SkIRect&); 90fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 911fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.comprivate: 921fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com typedef SkRGB16_Blitter INHERITED; 931fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com}; 941fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com 95867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com#ifdef USE_BLACK_BLITTER 961fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.comclass SkRGB16_Black_Blitter : public SkRGB16_Opaque_Blitter { 971fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.compublic: 981fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkRGB16_Black_Blitter(const SkBitmap& device, const SkPaint& paint); 991fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com virtual void blitMask(const SkMask&, const SkIRect&); 100a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com virtual void blitAntiH(int x, int y, const SkAlpha* antialias, 101a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com const int16_t* runs); 102fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 1031fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.comprivate: 1041fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com typedef SkRGB16_Opaque_Blitter INHERITED; 1051fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com}; 106867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com#endif 1071fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com 1081fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.comclass SkRGB16_Shader_Blitter : public SkShaderBlitter { 1091fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.compublic: 11087fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkRGB16_Shader_Blitter(const SkBitmap& device, const SkPaint& paint, 11187fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkShader::Context* shaderContext); 1121fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com virtual ~SkRGB16_Shader_Blitter(); 1131fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com virtual void blitH(int x, int y, int width); 114a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com virtual void blitAntiH(int x, int y, const SkAlpha* antialias, 115a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com const int16_t* runs); 1161fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com virtual void blitRect(int x, int y, int width, int height); 117fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 1181fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.comprotected: 1191fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkPMColor* fBuffer; 1201fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkBlitRow::Proc fOpaqueProc; 1211fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkBlitRow::Proc fAlphaProc; 122fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 1231fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.comprivate: 1241fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com // illegal 1251fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkRGB16_Shader_Blitter& operator=(const SkRGB16_Shader_Blitter&); 126fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 1271fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com typedef SkShaderBlitter INHERITED; 1281fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com}; 1291fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com 1301fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com// used only if the shader can perform shadSpan16 1311fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.comclass SkRGB16_Shader16_Blitter : public SkRGB16_Shader_Blitter { 1321fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.compublic: 13387fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkRGB16_Shader16_Blitter(const SkBitmap& device, const SkPaint& paint, 13487fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkShader::Context* shaderContext); 1351fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com virtual void blitH(int x, int y, int width); 136a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com virtual void blitAntiH(int x, int y, const SkAlpha* antialias, 137a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com const int16_t* runs); 1381fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com virtual void blitRect(int x, int y, int width, int height); 139fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 1401fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.comprivate: 1411fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com typedef SkRGB16_Shader_Blitter INHERITED; 1421fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com}; 1431fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com 1441fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.comclass SkRGB16_Shader_Xfermode_Blitter : public SkShaderBlitter { 1451fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.compublic: 14687fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkRGB16_Shader_Xfermode_Blitter(const SkBitmap& device, const SkPaint& paint, 14787fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkShader::Context* shaderContext); 1481fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com virtual ~SkRGB16_Shader_Xfermode_Blitter(); 1491fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com virtual void blitH(int x, int y, int width); 150a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com virtual void blitAntiH(int x, int y, const SkAlpha* antialias, 151a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com const int16_t* runs); 152fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 1531fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.comprivate: 1541fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkXfermode* fXfermode; 1551fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkPMColor* fBuffer; 1561fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com uint8_t* fAAExpand; 157fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 1581fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com // illegal 1591fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkRGB16_Shader_Xfermode_Blitter& operator=(const SkRGB16_Shader_Xfermode_Blitter&); 160fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 1611fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com typedef SkShaderBlitter INHERITED; 1621fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com}; 1631fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com 1641fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com/////////////////////////////////////////////////////////////////////////////// 165867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com#ifdef USE_BLACK_BLITTER 1668a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comSkRGB16_Black_Blitter::SkRGB16_Black_Blitter(const SkBitmap& device, const SkPaint& paint) 167dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com : INHERITED(device, paint) { 1688a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(paint.getShader() == NULL); 1698a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(paint.getColorFilter() == NULL); 1708a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(paint.getXfermode() == NULL); 1718a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(paint.getColor() == SK_ColorBLACK); 1728a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 1738a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 1748a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#if 1 1758a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#define black_8_pixels(mask, dst) \ 1768a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com do { \ 1778a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x80) dst[0] = 0; \ 1788a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x40) dst[1] = 0; \ 1798a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x20) dst[2] = 0; \ 1808a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x10) dst[3] = 0; \ 1818a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x08) dst[4] = 0; \ 1828a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x04) dst[5] = 0; \ 1838a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x02) dst[6] = 0; \ 1848a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x01) dst[7] = 0; \ 1858a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } while (0) 1868a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#else 1878a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comstatic inline black_8_pixels(U8CPU mask, uint16_t dst[]) 1888a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com{ 1898a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x80) dst[0] = 0; 1908a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x40) dst[1] = 0; 1918a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x20) dst[2] = 0; 1928a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x10) dst[3] = 0; 1938a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x08) dst[4] = 0; 1948a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x04) dst[5] = 0; 1958a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x02) dst[6] = 0; 1968a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask & 0x01) dst[7] = 0; 1978a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 1988a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#endif 1998a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 2008a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#define SK_BLITBWMASK_NAME SkRGB16_Black_BlitBW 2018a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#define SK_BLITBWMASK_ARGS 2028a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#define SK_BLITBWMASK_BLIT8(mask, dst) black_8_pixels(mask, dst) 2038a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#define SK_BLITBWMASK_GETADDR getAddr16 2048a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#define SK_BLITBWMASK_DEVTYPE uint16_t 2058a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#include "SkBlitBWMaskTemplate.h" 2068a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 207333d6cb2448d0febcbeb7c8c7310c0ff2d1a6104tomhudson@google.comvoid SkRGB16_Black_Blitter::blitMask(const SkMask& mask, 208333d6cb2448d0febcbeb7c8c7310c0ff2d1a6104tomhudson@google.com const SkIRect& clip) { 2098a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask.fFormat == SkMask::kBW_Format) { 2108a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkRGB16_Black_BlitBW(fDevice, mask, clip); 2118a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } else { 2128a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com uint16_t* SK_RESTRICT device = fDevice.getAddr16(clip.fLeft, clip.fTop); 2137989186dab6bc2f1c1927daf91bddd32b7fd8d0creed@google.com const uint8_t* SK_RESTRICT alpha = mask.getAddr8(clip.fLeft, clip.fTop); 2148a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com unsigned width = clip.width(); 2158a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com unsigned height = clip.height(); 216e5f48243bdbed2662be7a31be0888abc273b09e8scroggo@google.com size_t deviceRB = fDevice.rowBytes() - (width << 1); 2178a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com unsigned maskRB = mask.fRowBytes - width; 2188a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 2198a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT((int)height > 0); 2208a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT((int)width > 0); 2218a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT((int)deviceRB >= 0); 2228a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT((int)maskRB >= 0); 2238a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 2248a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com do { 2258a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com unsigned w = width; 2268a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com do { 2278a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com unsigned aa = *alpha++; 2288a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com *device = SkAlphaMulRGB16(*device, SkAlpha255To256(255 - aa)); 2298a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com device += 1; 2308a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } while (--w != 0); 2318a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com device = (uint16_t*)((char*)device + deviceRB); 2328a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com alpha += maskRB; 2338a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } while (--height != 0); 2348a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 2358a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 2368a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 2378a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comvoid SkRGB16_Black_Blitter::blitAntiH(int x, int y, 2388a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com const SkAlpha* SK_RESTRICT antialias, 239a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com const int16_t* SK_RESTRICT runs) { 2408a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com uint16_t* SK_RESTRICT device = fDevice.getAddr16(x, y); 2418a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 2428a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com for (;;) { 2438a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int count = runs[0]; 2448a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(count >= 0); 2458a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (count <= 0) { 2468a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com return; 2478a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 2488a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com runs += count; 2498a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 2508a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com unsigned aa = antialias[0]; 2518a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com antialias += count; 2528a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (aa) { 2538a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (aa == 255) { 2548a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com memset(device, 0, count << 1); 2558a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } else { 2568a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com aa = SkAlpha255To256(255 - aa); 2578a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com do { 2588a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com *device = SkAlphaMulRGB16(*device, aa); 2598a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com device += 1; 2608a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } while (--count != 0); 2618a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com continue; 2628a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 2638a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 2648a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com device += count; 2658a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 2668a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 267867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com#endif 2688a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 2699a74d313452f30629e2615eb8cbfe902433582c0reed@android.com/////////////////////////////////////////////////////////////////////////////// 2709a74d313452f30629e2615eb8cbfe902433582c0reed@android.com/////////////////////////////////////////////////////////////////////////////// 2719a74d313452f30629e2615eb8cbfe902433582c0reed@android.com 2729a74d313452f30629e2615eb8cbfe902433582c0reed@android.comSkRGB16_Opaque_Blitter::SkRGB16_Opaque_Blitter(const SkBitmap& device, 2739a74d313452f30629e2615eb8cbfe902433582c0reed@android.com const SkPaint& paint) 2749a74d313452f30629e2615eb8cbfe902433582c0reed@android.com: INHERITED(device, paint) {} 2759a74d313452f30629e2615eb8cbfe902433582c0reed@android.com 276a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.comvoid SkRGB16_Opaque_Blitter::blitH(int x, int y, int width) { 2779a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkASSERT(width > 0); 2789a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkASSERT(x + width <= fDevice.width()); 2799a74d313452f30629e2615eb8cbfe902433582c0reed@android.com uint16_t* SK_RESTRICT device = fDevice.getAddr16(x, y); 2809a74d313452f30629e2615eb8cbfe902433582c0reed@android.com uint16_t srcColor = fColor16; 28131d1c64bd54dd2b216846a30da4cc2e96765ec5freed@android.com 2829a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkASSERT(fRawColor16 == srcColor); 2839a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (fDoDither) { 2849a74d313452f30629e2615eb8cbfe902433582c0reed@android.com uint16_t ditherColor = fRawDither16; 2859a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if ((x ^ y) & 1) { 2869a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkTSwap(ditherColor, srcColor); 2879a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } 2889a74d313452f30629e2615eb8cbfe902433582c0reed@android.com sk_dither_memset16(device, srcColor, ditherColor, width); 2899a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } else { 2909a74d313452f30629e2615eb8cbfe902433582c0reed@android.com sk_memset16(device, srcColor, width); 2919a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } 2929a74d313452f30629e2615eb8cbfe902433582c0reed@android.com} 2939a74d313452f30629e2615eb8cbfe902433582c0reed@android.com 2949a74d313452f30629e2615eb8cbfe902433582c0reed@android.com// return 1 or 0 from a bool 29563debae4c1020fa1e0ccd92ef3cbfdc8735acf8ereed@android.comstatic inline int Bool2Int(int value) { 296fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com return !!value; 2979a74d313452f30629e2615eb8cbfe902433582c0reed@android.com} 2989a74d313452f30629e2615eb8cbfe902433582c0reed@android.com 2999a74d313452f30629e2615eb8cbfe902433582c0reed@android.comvoid SkRGB16_Opaque_Blitter::blitAntiH(int x, int y, 3009a74d313452f30629e2615eb8cbfe902433582c0reed@android.com const SkAlpha* SK_RESTRICT antialias, 301a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com const int16_t* SK_RESTRICT runs) { 3029a74d313452f30629e2615eb8cbfe902433582c0reed@android.com uint16_t* SK_RESTRICT device = fDevice.getAddr16(x, y); 3039a74d313452f30629e2615eb8cbfe902433582c0reed@android.com uint16_t srcColor = fRawColor16; 304ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com uint32_t srcExpanded = fExpandedRaw16; 3059a74d313452f30629e2615eb8cbfe902433582c0reed@android.com int ditherInt = Bool2Int(fDoDither); 3069a74d313452f30629e2615eb8cbfe902433582c0reed@android.com uint16_t ditherColor = fRawDither16; 3079a74d313452f30629e2615eb8cbfe902433582c0reed@android.com // if we have no dithering, this will always fail 3089a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if ((x ^ y) & ditherInt) { 3099a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkTSwap(ditherColor, srcColor); 3109a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } 3119a74d313452f30629e2615eb8cbfe902433582c0reed@android.com for (;;) { 3129a74d313452f30629e2615eb8cbfe902433582c0reed@android.com int count = runs[0]; 3139a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkASSERT(count >= 0); 3149a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (count <= 0) { 3159a74d313452f30629e2615eb8cbfe902433582c0reed@android.com return; 3169a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } 3179a74d313452f30629e2615eb8cbfe902433582c0reed@android.com runs += count; 31831d1c64bd54dd2b216846a30da4cc2e96765ec5freed@android.com 3199a74d313452f30629e2615eb8cbfe902433582c0reed@android.com unsigned aa = antialias[0]; 3209a74d313452f30629e2615eb8cbfe902433582c0reed@android.com antialias += count; 3219a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (aa) { 3229a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (aa == 255) { 3239a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (ditherInt) { 3249a74d313452f30629e2615eb8cbfe902433582c0reed@android.com sk_dither_memset16(device, srcColor, 3259a74d313452f30629e2615eb8cbfe902433582c0reed@android.com ditherColor, count); 3269a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } else { 3279a74d313452f30629e2615eb8cbfe902433582c0reed@android.com sk_memset16(device, srcColor, count); 3289a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } 3299a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } else { 3309a74d313452f30629e2615eb8cbfe902433582c0reed@android.com // TODO: respect fDoDither 3319a74d313452f30629e2615eb8cbfe902433582c0reed@android.com unsigned scale5 = SkAlpha255To256(aa) >> 3; 332ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com uint32_t src32 = srcExpanded * scale5; 3339a74d313452f30629e2615eb8cbfe902433582c0reed@android.com scale5 = 32 - scale5; // now we can use it on the device 3349a74d313452f30629e2615eb8cbfe902433582c0reed@android.com int n = count; 3359a74d313452f30629e2615eb8cbfe902433582c0reed@android.com do { 3369a74d313452f30629e2615eb8cbfe902433582c0reed@android.com uint32_t dst32 = SkExpand_rgb_16(*device) * scale5; 3379a74d313452f30629e2615eb8cbfe902433582c0reed@android.com *device++ = SkCompact_rgb_16((src32 + dst32) >> 5); 3389a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } while (--n != 0); 3399a74d313452f30629e2615eb8cbfe902433582c0reed@android.com goto DONE; 3409a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } 3419a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } 3429a74d313452f30629e2615eb8cbfe902433582c0reed@android.com device += count; 34331d1c64bd54dd2b216846a30da4cc2e96765ec5freed@android.com 3449a74d313452f30629e2615eb8cbfe902433582c0reed@android.com DONE: 3459a74d313452f30629e2615eb8cbfe902433582c0reed@android.com // if we have no dithering, this will always fail 3469a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (count & ditherInt) { 3479a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkTSwap(ditherColor, srcColor); 3489a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } 3499a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } 3509a74d313452f30629e2615eb8cbfe902433582c0reed@android.com} 3519a74d313452f30629e2615eb8cbfe902433582c0reed@android.com 3529a74d313452f30629e2615eb8cbfe902433582c0reed@android.com#define solid_8_pixels(mask, dst, color) \ 3539a74d313452f30629e2615eb8cbfe902433582c0reed@android.com do { \ 3549a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (mask & 0x80) dst[0] = color; \ 3559a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (mask & 0x40) dst[1] = color; \ 3569a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (mask & 0x20) dst[2] = color; \ 3579a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (mask & 0x10) dst[3] = color; \ 3589a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (mask & 0x08) dst[4] = color; \ 3599a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (mask & 0x04) dst[5] = color; \ 3609a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (mask & 0x02) dst[6] = color; \ 3619a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (mask & 0x01) dst[7] = color; \ 3629a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } while (0) 3639a74d313452f30629e2615eb8cbfe902433582c0reed@android.com 3649a74d313452f30629e2615eb8cbfe902433582c0reed@android.com#define SK_BLITBWMASK_NAME SkRGB16_BlitBW 3659a74d313452f30629e2615eb8cbfe902433582c0reed@android.com#define SK_BLITBWMASK_ARGS , uint16_t color 3669a74d313452f30629e2615eb8cbfe902433582c0reed@android.com#define SK_BLITBWMASK_BLIT8(mask, dst) solid_8_pixels(mask, dst, color) 3679a74d313452f30629e2615eb8cbfe902433582c0reed@android.com#define SK_BLITBWMASK_GETADDR getAddr16 3689a74d313452f30629e2615eb8cbfe902433582c0reed@android.com#define SK_BLITBWMASK_DEVTYPE uint16_t 3699a74d313452f30629e2615eb8cbfe902433582c0reed@android.com#include "SkBlitBWMaskTemplate.h" 3709a74d313452f30629e2615eb8cbfe902433582c0reed@android.com 3719a74d313452f30629e2615eb8cbfe902433582c0reed@android.comstatic U16CPU blend_compact(uint32_t src32, uint32_t dst32, unsigned scale5) { 3729a74d313452f30629e2615eb8cbfe902433582c0reed@android.com return SkCompact_rgb_16(dst32 + ((src32 - dst32) * scale5 >> 5)); 3739a74d313452f30629e2615eb8cbfe902433582c0reed@android.com} 3749a74d313452f30629e2615eb8cbfe902433582c0reed@android.com 375333d6cb2448d0febcbeb7c8c7310c0ff2d1a6104tomhudson@google.comvoid SkRGB16_Opaque_Blitter::blitMask(const SkMask& mask, 376333d6cb2448d0febcbeb7c8c7310c0ff2d1a6104tomhudson@google.com const SkIRect& clip) { 3779a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (mask.fFormat == SkMask::kBW_Format) { 3789a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkRGB16_BlitBW(fDevice, mask, clip, fColor16); 3799a74d313452f30629e2615eb8cbfe902433582c0reed@android.com return; 3809a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } 38131d1c64bd54dd2b216846a30da4cc2e96765ec5freed@android.com 3829a74d313452f30629e2615eb8cbfe902433582c0reed@android.com uint16_t* SK_RESTRICT device = fDevice.getAddr16(clip.fLeft, clip.fTop); 3837989186dab6bc2f1c1927daf91bddd32b7fd8d0creed@google.com const uint8_t* SK_RESTRICT alpha = mask.getAddr8(clip.fLeft, clip.fTop); 3849a74d313452f30629e2615eb8cbfe902433582c0reed@android.com int width = clip.width(); 3859a74d313452f30629e2615eb8cbfe902433582c0reed@android.com int height = clip.height(); 386e5f48243bdbed2662be7a31be0888abc273b09e8scroggo@google.com size_t deviceRB = fDevice.rowBytes() - (width << 1); 3879a74d313452f30629e2615eb8cbfe902433582c0reed@android.com unsigned maskRB = mask.fRowBytes - width; 388ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com uint32_t expanded32 = fExpandedRaw16; 38931d1c64bd54dd2b216846a30da4cc2e96765ec5freed@android.com 39089351ec35a05eaf59edb7431d23a754cd084a363commit-bot@chromium.org#if SK_ARM_NEON_IS_ALWAYS && defined(SK_CPU_LENDIAN) 391fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com#define UNROLL 8 392867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com do { 393867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com int w = width; 394867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com if (w >= UNROLL) { 395641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org uint32x4_t color, dev_lo, dev_hi; 396641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org uint32x4_t wn1, wn2, tmp; 397641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org uint32x4_t vmask_g16, vmask_ng16; 398641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org uint16x8_t valpha, vdev; 399641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org uint16x4_t odev_lo, odev_hi, valpha_lo, valpha_hi; 400641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org 401641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org // prepare constants 402641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org vmask_g16 = vdupq_n_u32(SK_G16_MASK_IN_PLACE); 403641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org vmask_ng16 = vdupq_n_u32(~SK_G16_MASK_IN_PLACE); 404867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com color = vdupq_n_u32(expanded32); 405fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 406867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com do { 407641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org // alpha is 8x8, widen and split to get a pair of 16x4 408641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org valpha = vaddw_u8(vdupq_n_u16(1), vld1_u8(alpha)); 409641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org valpha = vshrq_n_u16(valpha, 3); 410641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org valpha_lo = vget_low_u16(valpha); 411641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org valpha_hi = vget_high_u16(valpha); 412641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org 413641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org // load pixels 414641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org vdev = vld1q_u16(device); 415641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org dev_lo = vmovl_u16(vget_low_u16(vdev)); 416641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org dev_hi = vmovl_u16(vget_high_u16(vdev)); 417641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org 418641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org // unpack them in 32 bits 419641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org dev_lo = (dev_lo & vmask_ng16) | vshlq_n_u32(dev_lo & vmask_g16, 16); 420641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org dev_hi = (dev_hi & vmask_ng16) | vshlq_n_u32(dev_hi & vmask_g16, 16); 421641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org 422641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org // blend with color 423641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org tmp = (color - dev_lo) * vmovl_u16(valpha_lo); 424641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org tmp = vshrq_n_u32(tmp, 5); 425641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org dev_lo += tmp; 426641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org 427641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org tmp = vmulq_u32(color - dev_hi, vmovl_u16(valpha_hi)); 428641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org tmp = vshrq_n_u32(tmp, 5); 429641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org dev_hi += tmp; 430641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org 431641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org // re-compact 432641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org wn1 = dev_lo & vmask_ng16; 433641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org wn2 = vshrq_n_u32(dev_lo, 16) & vmask_g16; 434641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org odev_lo = vmovn_u32(wn1 | wn2); 435641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org 436641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org wn1 = dev_hi & vmask_ng16; 437641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org wn2 = vshrq_n_u32(dev_hi, 16) & vmask_g16; 438641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org odev_hi = vmovn_u32(wn1 | wn2); 439641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org 440641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org // store 441641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org vst1q_u16(device, vcombine_u16(odev_lo, odev_hi)); 442fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 443867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com device += UNROLL; 444867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com alpha += UNROLL; 445867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com w -= UNROLL; 446867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com } while (w >= UNROLL); 447867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com } 448fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 449641a2491964f7e5921fad6649be08175e03b0434commit-bot@chromium.org // residuals 450867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com while (w > 0) { 451867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com *device = blend_compact(expanded32, SkExpand_rgb_16(*device), 452867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com SkAlpha255To256(*alpha++) >> 3); 453867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com device += 1; 454867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com --w; 455867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com } 456867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com device = (uint16_t*)((char*)device + deviceRB); 457867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com alpha += maskRB; 458867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com } while (--height != 0); 459fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com#undef UNROLL 460867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com#else // non-neon code 4619a74d313452f30629e2615eb8cbfe902433582c0reed@android.com do { 4629a74d313452f30629e2615eb8cbfe902433582c0reed@android.com int w = width; 4639a74d313452f30629e2615eb8cbfe902433582c0reed@android.com do { 464ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com *device = blend_compact(expanded32, SkExpand_rgb_16(*device), 4659a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkAlpha255To256(*alpha++) >> 3); 4669a74d313452f30629e2615eb8cbfe902433582c0reed@android.com device += 1; 4679a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } while (--w != 0); 4689a74d313452f30629e2615eb8cbfe902433582c0reed@android.com device = (uint16_t*)((char*)device + deviceRB); 4699a74d313452f30629e2615eb8cbfe902433582c0reed@android.com alpha += maskRB; 4709a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } while (--height != 0); 471867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com#endif 4729a74d313452f30629e2615eb8cbfe902433582c0reed@android.com} 4739a74d313452f30629e2615eb8cbfe902433582c0reed@android.com 474ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.comvoid SkRGB16_Opaque_Blitter::blitV(int x, int y, int height, SkAlpha alpha) { 475ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com uint16_t* SK_RESTRICT device = fDevice.getAddr16(x, y); 476e5f48243bdbed2662be7a31be0888abc273b09e8scroggo@google.com size_t deviceRB = fDevice.rowBytes(); 477fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 478ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com // TODO: respect fDoDither 479ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com unsigned scale5 = SkAlpha255To256(alpha) >> 3; 480ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com uint32_t src32 = fExpandedRaw16 * scale5; 481ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com scale5 = 32 - scale5; 482ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com do { 483ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com uint32_t dst32 = SkExpand_rgb_16(*device) * scale5; 484ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com *device = SkCompact_rgb_16((src32 + dst32) >> 5); 485ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com device = (uint16_t*)((char*)device + deviceRB); 486ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com } while (--height != 0); 487ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com} 488ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com 4899a74d313452f30629e2615eb8cbfe902433582c0reed@android.comvoid SkRGB16_Opaque_Blitter::blitRect(int x, int y, int width, int height) { 4909a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkASSERT(x + width <= fDevice.width() && y + height <= fDevice.height()); 4919a74d313452f30629e2615eb8cbfe902433582c0reed@android.com uint16_t* SK_RESTRICT device = fDevice.getAddr16(x, y); 492e5f48243bdbed2662be7a31be0888abc273b09e8scroggo@google.com size_t deviceRB = fDevice.rowBytes(); 4939a74d313452f30629e2615eb8cbfe902433582c0reed@android.com uint16_t color16 = fColor16; 49431d1c64bd54dd2b216846a30da4cc2e96765ec5freed@android.com 4959a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (fDoDither) { 4969a74d313452f30629e2615eb8cbfe902433582c0reed@android.com uint16_t ditherColor = fRawDither16; 4979a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if ((x ^ y) & 1) { 4989a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkTSwap(ditherColor, color16); 4999a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } 5009a74d313452f30629e2615eb8cbfe902433582c0reed@android.com while (--height >= 0) { 5019a74d313452f30629e2615eb8cbfe902433582c0reed@android.com sk_dither_memset16(device, color16, ditherColor, width); 5029a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkTSwap(ditherColor, color16); 5039a74d313452f30629e2615eb8cbfe902433582c0reed@android.com device = (uint16_t*)((char*)device + deviceRB); 5049a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } 5059a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } else { // no dither 5069a74d313452f30629e2615eb8cbfe902433582c0reed@android.com while (--height >= 0) { 5079a74d313452f30629e2615eb8cbfe902433582c0reed@android.com sk_memset16(device, color16, width); 5089a74d313452f30629e2615eb8cbfe902433582c0reed@android.com device = (uint16_t*)((char*)device + deviceRB); 5099a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } 5109a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } 5119a74d313452f30629e2615eb8cbfe902433582c0reed@android.com} 5129a74d313452f30629e2615eb8cbfe902433582c0reed@android.com 5139a74d313452f30629e2615eb8cbfe902433582c0reed@android.com/////////////////////////////////////////////////////////////////////////////// 5148a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 5158a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comSkRGB16_Blitter::SkRGB16_Blitter(const SkBitmap& device, const SkPaint& paint) 5168a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com : INHERITED(device) { 5178a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkColor color = paint.getColor(); 5188a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 5198a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com fSrcColor32 = SkPreMultiplyColor(color); 5208a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com fScale = SkAlpha255To256(SkColorGetA(color)); 5218a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 5228a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int r = SkColorGetR(color); 5238a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int g = SkColorGetG(color); 5248a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int b = SkColorGetB(color); 5258a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 5268a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com fRawColor16 = fRawDither16 = SkPack888ToRGB16(r, g, b); 5278a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com // if we're dithered, use fRawDither16 to hold that. 5288a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if ((fDoDither = paint.isDither()) != false) { 5298a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com fRawDither16 = SkDitherPack888ToRGB16(r, g, b); 5308a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 531ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com 532ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com fExpandedRaw16 = SkExpand_rgb_16(fRawColor16); 533ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com 5348a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com fColor16 = SkPackRGB16( SkAlphaMul(r, fScale) >> (8 - SK_R16_BITS), 5358a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkAlphaMul(g, fScale) >> (8 - SK_G16_BITS), 5368a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkAlphaMul(b, fScale) >> (8 - SK_B16_BITS)); 5378a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 5388a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 5398a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comconst SkBitmap* SkRGB16_Blitter::justAnOpaqueColor(uint32_t* value) { 5408a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (!fDoDither && 256 == fScale) { 5418a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com *value = fRawColor16; 5428a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com return &fDevice; 5438a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 5448a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com return NULL; 5458a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 5468a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 547dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.comstatic uint32_t pmcolor_to_expand16(SkPMColor c) { 548dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com unsigned r = SkGetPackedR32(c); 549dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com unsigned g = SkGetPackedG32(c); 550dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com unsigned b = SkGetPackedB32(c); 551dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com return (g << 24) | (r << 13) | (b << 2); 552dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com} 553dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com 554dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.comstatic inline void blend32_16_row(SkPMColor src, uint16_t dst[], int count) { 555dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com SkASSERT(count > 0); 556dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com uint32_t src_expand = pmcolor_to_expand16(src); 557b602b8e5334edc0bfcdf086c2ea58e2b5d5f1f3breed@android.com unsigned scale = SkAlpha255To256(0xFF - SkGetPackedA32(src)) >> 3; 558dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com do { 559dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com uint32_t dst_expand = SkExpand_rgb_16(*dst) * scale; 560dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com *dst = SkCompact_rgb_16((src_expand + dst_expand) >> 5); 561dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com dst += 1; 562dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com } while (--count != 0); 563dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com} 564dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com 565a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.comvoid SkRGB16_Blitter::blitH(int x, int y, int width) { 5668a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(width > 0); 5678a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(x + width <= fDevice.width()); 5688a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com uint16_t* SK_RESTRICT device = fDevice.getAddr16(x, y); 5698a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 5709a74d313452f30629e2615eb8cbfe902433582c0reed@android.com // TODO: respect fDoDither 571dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com blend32_16_row(fSrcColor32, device, width); 5728a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 5738a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 5748a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comvoid SkRGB16_Blitter::blitAntiH(int x, int y, 5758a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com const SkAlpha* SK_RESTRICT antialias, 576a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com const int16_t* SK_RESTRICT runs) { 5778a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com uint16_t* SK_RESTRICT device = fDevice.getAddr16(x, y); 578ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com uint32_t srcExpanded = fExpandedRaw16; 5798a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com unsigned scale = fScale; 5808a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 5819a74d313452f30629e2615eb8cbfe902433582c0reed@android.com // TODO: respect fDoDither 5829a74d313452f30629e2615eb8cbfe902433582c0reed@android.com for (;;) { 5839a74d313452f30629e2615eb8cbfe902433582c0reed@android.com int count = runs[0]; 5849a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkASSERT(count >= 0); 5859a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (count <= 0) { 5869a74d313452f30629e2615eb8cbfe902433582c0reed@android.com return; 5878a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 5889a74d313452f30629e2615eb8cbfe902433582c0reed@android.com runs += count; 5898a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 5909a74d313452f30629e2615eb8cbfe902433582c0reed@android.com unsigned aa = antialias[0]; 5919a74d313452f30629e2615eb8cbfe902433582c0reed@android.com antialias += count; 5929a74d313452f30629e2615eb8cbfe902433582c0reed@android.com if (aa) { 5939a74d313452f30629e2615eb8cbfe902433582c0reed@android.com unsigned scale5 = SkAlpha255To256(aa) * scale >> (8 + 3); 594ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com uint32_t src32 = srcExpanded * scale5; 5959a74d313452f30629e2615eb8cbfe902433582c0reed@android.com scale5 = 32 - scale5; 5969a74d313452f30629e2615eb8cbfe902433582c0reed@android.com do { 5979a74d313452f30629e2615eb8cbfe902433582c0reed@android.com uint32_t dst32 = SkExpand_rgb_16(*device) * scale5; 5989a74d313452f30629e2615eb8cbfe902433582c0reed@android.com *device++ = SkCompact_rgb_16((src32 + dst32) >> 5); 5999a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } while (--count != 0); 6009a74d313452f30629e2615eb8cbfe902433582c0reed@android.com continue; 6018a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 6029a74d313452f30629e2615eb8cbfe902433582c0reed@android.com device += count; 6038a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 6048a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 6058a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 6068a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comstatic inline void blend_8_pixels(U8CPU bw, uint16_t dst[], unsigned dst_scale, 6078a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com U16CPU srcColor) { 6088a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (bw & 0x80) dst[0] = srcColor + SkAlphaMulRGB16(dst[0], dst_scale); 6098a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (bw & 0x40) dst[1] = srcColor + SkAlphaMulRGB16(dst[1], dst_scale); 6108a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (bw & 0x20) dst[2] = srcColor + SkAlphaMulRGB16(dst[2], dst_scale); 6118a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (bw & 0x10) dst[3] = srcColor + SkAlphaMulRGB16(dst[3], dst_scale); 6128a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (bw & 0x08) dst[4] = srcColor + SkAlphaMulRGB16(dst[4], dst_scale); 6138a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (bw & 0x04) dst[5] = srcColor + SkAlphaMulRGB16(dst[5], dst_scale); 6148a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (bw & 0x02) dst[6] = srcColor + SkAlphaMulRGB16(dst[6], dst_scale); 6158a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (bw & 0x01) dst[7] = srcColor + SkAlphaMulRGB16(dst[7], dst_scale); 6168a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 6178a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 6188a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#define SK_BLITBWMASK_NAME SkRGB16_BlendBW 6198a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#define SK_BLITBWMASK_ARGS , unsigned dst_scale, U16CPU src_color 6208a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#define SK_BLITBWMASK_BLIT8(mask, dst) blend_8_pixels(mask, dst, dst_scale, src_color) 6218a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#define SK_BLITBWMASK_GETADDR getAddr16 6228a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#define SK_BLITBWMASK_DEVTYPE uint16_t 6238a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com#include "SkBlitBWMaskTemplate.h" 6248a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 625333d6cb2448d0febcbeb7c8c7310c0ff2d1a6104tomhudson@google.comvoid SkRGB16_Blitter::blitMask(const SkMask& mask, 626333d6cb2448d0febcbeb7c8c7310c0ff2d1a6104tomhudson@google.com const SkIRect& clip) { 6278a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (mask.fFormat == SkMask::kBW_Format) { 6289a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkRGB16_BlendBW(fDevice, mask, clip, 256 - fScale, fColor16); 6298a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com return; 6308a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 6318a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 6328a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com uint16_t* SK_RESTRICT device = fDevice.getAddr16(clip.fLeft, clip.fTop); 6337989186dab6bc2f1c1927daf91bddd32b7fd8d0creed@google.com const uint8_t* SK_RESTRICT alpha = mask.getAddr8(clip.fLeft, clip.fTop); 6348a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int width = clip.width(); 6358a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int height = clip.height(); 636e5f48243bdbed2662be7a31be0888abc273b09e8scroggo@google.com size_t deviceRB = fDevice.rowBytes() - (width << 1); 6378a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com unsigned maskRB = mask.fRowBytes - width; 638ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com uint32_t color32 = fExpandedRaw16; 6398a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 6409a74d313452f30629e2615eb8cbfe902433582c0reed@android.com unsigned scale256 = fScale; 6419a74d313452f30629e2615eb8cbfe902433582c0reed@android.com do { 6429a74d313452f30629e2615eb8cbfe902433582c0reed@android.com int w = width; 6438a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com do { 6449a74d313452f30629e2615eb8cbfe902433582c0reed@android.com unsigned aa = *alpha++; 6459a74d313452f30629e2615eb8cbfe902433582c0reed@android.com unsigned scale = SkAlpha255To256(aa) * scale256 >> (8 + 3); 6469a74d313452f30629e2615eb8cbfe902433582c0reed@android.com uint32_t src32 = color32 * scale; 6479a74d313452f30629e2615eb8cbfe902433582c0reed@android.com uint32_t dst32 = SkExpand_rgb_16(*device) * (32 - scale); 6489a74d313452f30629e2615eb8cbfe902433582c0reed@android.com *device++ = SkCompact_rgb_16((src32 + dst32) >> 5); 6499a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } while (--w != 0); 6509a74d313452f30629e2615eb8cbfe902433582c0reed@android.com device = (uint16_t*)((char*)device + deviceRB); 6519a74d313452f30629e2615eb8cbfe902433582c0reed@android.com alpha += maskRB; 6529a74d313452f30629e2615eb8cbfe902433582c0reed@android.com } while (--height != 0); 6538a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 6548a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 6558a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comvoid SkRGB16_Blitter::blitV(int x, int y, int height, SkAlpha alpha) { 6568a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com uint16_t* SK_RESTRICT device = fDevice.getAddr16(x, y); 657e5f48243bdbed2662be7a31be0888abc273b09e8scroggo@google.com size_t deviceRB = fDevice.rowBytes(); 6588a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 659ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com // TODO: respect fDoDither 660ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com unsigned scale5 = SkAlpha255To256(alpha) * fScale >> (8 + 3); 661ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com uint32_t src32 = fExpandedRaw16 * scale5; 662ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com scale5 = 32 - scale5; 663ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com do { 664ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com uint32_t dst32 = SkExpand_rgb_16(*device) * scale5; 665ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com *device = SkCompact_rgb_16((src32 + dst32) >> 5); 666ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com device = (uint16_t*)((char*)device + deviceRB); 667ea16cfa037bca933f6930a487b42f3c0faab9fe4reed@android.com } while (--height != 0); 6688a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 6698a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 6708a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comvoid SkRGB16_Blitter::blitRect(int x, int y, int width, int height) { 6718a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(x + width <= fDevice.width() && y + height <= fDevice.height()); 6728a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com uint16_t* SK_RESTRICT device = fDevice.getAddr16(x, y); 673e5f48243bdbed2662be7a31be0888abc273b09e8scroggo@google.com size_t deviceRB = fDevice.rowBytes(); 6749a74d313452f30629e2615eb8cbfe902433582c0reed@android.com SkPMColor src32 = fSrcColor32; 6758a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 6769a74d313452f30629e2615eb8cbfe902433582c0reed@android.com while (--height >= 0) { 677dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com blend32_16_row(src32, device, width); 6789a74d313452f30629e2615eb8cbfe902433582c0reed@android.com device = (uint16_t*)((char*)device + deviceRB); 6798a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 6808a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 6818a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 6828a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com/////////////////////////////////////////////////////////////////////////////// 6838a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 6848a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comSkRGB16_Shader16_Blitter::SkRGB16_Shader16_Blitter(const SkBitmap& device, 68587fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org const SkPaint& paint, 68687fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkShader::Context* shaderContext) 68787fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org : SkRGB16_Shader_Blitter(device, paint, shaderContext) { 6885119bdb952025a30f115b9c6a187173956e55097reed@android.com SkASSERT(SkShader::CanCallShadeSpan16(fShaderFlags)); 6898a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 6908a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 691a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.comvoid SkRGB16_Shader16_Blitter::blitH(int x, int y, int width) { 6928a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(x + width <= fDevice.width()); 6938a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 6948a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com uint16_t* SK_RESTRICT device = fDevice.getAddr16(x, y); 69587fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkShader::Context* shaderContext = fShaderContext; 6968a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 69787fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org int alpha = shaderContext->getSpan16Alpha(); 6988a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (0xFF == alpha) { 69987fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org shaderContext->shadeSpan16(x, y, device, width); 7008a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } else { 7018a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com uint16_t* span16 = (uint16_t*)fBuffer; 70287fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org shaderContext->shadeSpan16(x, y, span16, width); 7038a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkBlendRGB16(span16, device, SkAlpha255To256(alpha), width); 7048a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 7058a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 7068a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 707dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.comvoid SkRGB16_Shader16_Blitter::blitRect(int x, int y, int width, int height) { 70887fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkShader::Context* shaderContext = fShaderContext; 70987fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org uint16_t* dst = fDevice.getAddr16(x, y); 71087fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org size_t dstRB = fDevice.rowBytes(); 71187fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org int alpha = shaderContext->getSpan16Alpha(); 712dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com 713dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com if (0xFF == alpha) { 7143c9b2a4a0e4f57db23640e85959ee78b86634628reed@android.com if (fShaderFlags & SkShader::kConstInY16_Flag) { 715dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com // have the shader blit directly into the device the first time 71687fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org shaderContext->shadeSpan16(x, y, dst, width); 717dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com // and now just memcpy that line on the subsequent lines 718dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com if (--height > 0) { 719dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com const uint16_t* orig = dst; 720dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com do { 721dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com dst = (uint16_t*)((char*)dst + dstRB); 722dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com memcpy(dst, orig, width << 1); 723dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com } while (--height); 724dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com } 725dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com } else { // need to call shadeSpan16 for every line 726dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com do { 72787fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org shaderContext->shadeSpan16(x, y, dst, width); 728dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com y += 1; 729dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com dst = (uint16_t*)((char*)dst + dstRB); 730dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com } while (--height); 731dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com } 732dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com } else { 733dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com int scale = SkAlpha255To256(alpha); 734dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com uint16_t* span16 = (uint16_t*)fBuffer; 7353c9b2a4a0e4f57db23640e85959ee78b86634628reed@android.com if (fShaderFlags & SkShader::kConstInY16_Flag) { 73687fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org shaderContext->shadeSpan16(x, y, span16, width); 737dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com do { 738dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com SkBlendRGB16(span16, dst, scale, width); 739dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com dst = (uint16_t*)((char*)dst + dstRB); 740dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com } while (--height); 741dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com } else { 742dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com do { 74387fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org shaderContext->shadeSpan16(x, y, span16, width); 744dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com SkBlendRGB16(span16, dst, scale, width); 745dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com y += 1; 746dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com dst = (uint16_t*)((char*)dst + dstRB); 747dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com } while (--height); 748dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com } 749dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com } 750dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com} 751dafaf7ac4d89f183dc515907665cdac3e3098466reed@android.com 7528a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comvoid SkRGB16_Shader16_Blitter::blitAntiH(int x, int y, 7538a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com const SkAlpha* SK_RESTRICT antialias, 754a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com const int16_t* SK_RESTRICT runs) { 75587fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkShader::Context* shaderContext = fShaderContext; 7568a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkPMColor* SK_RESTRICT span = fBuffer; 75787fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org uint16_t* SK_RESTRICT device = fDevice.getAddr16(x, y); 7588a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 75987fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org int alpha = shaderContext->getSpan16Alpha(); 7608a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com uint16_t* span16 = (uint16_t*)span; 7618a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 7628a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (0xFF == alpha) { 7638a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com for (;;) { 7648a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int count = *runs; 7658a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (count <= 0) { 7668a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com break; 7678a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 7688a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(count <= fDevice.width()); // don't overrun fBuffer 7698a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 7708a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int aa = *antialias; 7718a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (aa == 255) { 7728a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com // go direct to the device! 77387fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org shaderContext->shadeSpan16(x, y, device, count); 7748a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } else if (aa) { 77587fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org shaderContext->shadeSpan16(x, y, span16, count); 7768a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkBlendRGB16(span16, device, SkAlpha255To256(aa), count); 7778a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 7788a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com device += count; 7798a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com runs += count; 7808a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com antialias += count; 7818a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com x += count; 7828a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 7838a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } else { // span alpha is < 255 7848a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com alpha = SkAlpha255To256(alpha); 7858a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com for (;;) { 7868a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int count = *runs; 7878a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (count <= 0) { 7888a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com break; 7898a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 7908a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(count <= fDevice.width()); // don't overrun fBuffer 7918a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 7928a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int aa = SkAlphaMul(*antialias, alpha); 7938a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (aa) { 79487fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org shaderContext->shadeSpan16(x, y, span16, count); 7958a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkBlendRGB16(span16, device, SkAlpha255To256(aa), count); 7968a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 7978a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 7988a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com device += count; 7998a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com runs += count; 8008a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com antialias += count; 8018a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com x += count; 8028a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 8038a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 8048a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 8058a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 8068a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com/////////////////////////////////////////////////////////////////////////////// 8078a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 8088a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comSkRGB16_Shader_Blitter::SkRGB16_Shader_Blitter(const SkBitmap& device, 80987fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org const SkPaint& paint, 81087fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkShader::Context* shaderContext) 81187fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org: INHERITED(device, paint, shaderContext) { 8128a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(paint.getXfermode() == NULL); 8138a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 8148a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com fBuffer = (SkPMColor*)sk_malloc_throw(device.width() * sizeof(SkPMColor)); 8158a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 8168a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com // compute SkBlitRow::Procs 8178a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com unsigned flags = 0; 818fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 8195119bdb952025a30f115b9c6a187173956e55097reed@android.com uint32_t shaderFlags = fShaderFlags; 8208a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com // shaders take care of global alpha, so we never set it in SkBlitRow 8218a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (!(shaderFlags & SkShader::kOpaqueAlpha_Flag)) { 8228a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com flags |= SkBlitRow::kSrcPixelAlpha_Flag; 823c2050e3a3ecfb8738b36e2add15c526e8e0f21fecommit-bot@chromium.org } 8248a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com // don't dither if the shader is really 16bit 8258a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (paint.isDither() && !(shaderFlags & SkShader::kIntrinsicly16_Flag)) { 8268a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com flags |= SkBlitRow::kDither_Flag; 8278a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 8288a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com // used when we know our global alpha is 0xFF 829cba73780bbd12fd254229517aec04fcbf0b64b52commit-bot@chromium.org fOpaqueProc = SkBlitRow::Factory(flags, kRGB_565_SkColorType); 8308a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com // used when we know our global alpha is < 0xFF 8318a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com fAlphaProc = SkBlitRow::Factory(flags | SkBlitRow::kGlobalAlpha_Flag, 832cba73780bbd12fd254229517aec04fcbf0b64b52commit-bot@chromium.org kRGB_565_SkColorType); 8338a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 8348a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 8358a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comSkRGB16_Shader_Blitter::~SkRGB16_Shader_Blitter() { 8368a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com sk_free(fBuffer); 8378a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 8388a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 8398a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comvoid SkRGB16_Shader_Blitter::blitH(int x, int y, int width) { 8408a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(x + width <= fDevice.width()); 8418a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 84287fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org fShaderContext->shadeSpan(x, y, fBuffer, width); 8438a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com // shaders take care of global alpha, so we pass 0xFF (should be ignored) 8448a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com fOpaqueProc(fDevice.getAddr16(x, y), fBuffer, width, 0xFF, x, y); 8458a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 8468a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 8475119bdb952025a30f115b9c6a187173956e55097reed@android.comvoid SkRGB16_Shader_Blitter::blitRect(int x, int y, int width, int height) { 84887fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkShader::Context* shaderContext = fShaderContext; 84987fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkBlitRow::Proc proc = fOpaqueProc; 85087fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkPMColor* buffer = fBuffer; 85187fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org uint16_t* dst = fDevice.getAddr16(x, y); 85287fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org size_t dstRB = fDevice.rowBytes(); 8535119bdb952025a30f115b9c6a187173956e55097reed@android.com 8543c9b2a4a0e4f57db23640e85959ee78b86634628reed@android.com if (fShaderFlags & SkShader::kConstInY32_Flag) { 85587fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org shaderContext->shadeSpan(x, y, buffer, width); 8565119bdb952025a30f115b9c6a187173956e55097reed@android.com do { 8575119bdb952025a30f115b9c6a187173956e55097reed@android.com proc(dst, buffer, width, 0xFF, x, y); 8585119bdb952025a30f115b9c6a187173956e55097reed@android.com y += 1; 8595119bdb952025a30f115b9c6a187173956e55097reed@android.com dst = (uint16_t*)((char*)dst + dstRB); 8605119bdb952025a30f115b9c6a187173956e55097reed@android.com } while (--height); 8615119bdb952025a30f115b9c6a187173956e55097reed@android.com } else { 8625119bdb952025a30f115b9c6a187173956e55097reed@android.com do { 86387fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org shaderContext->shadeSpan(x, y, buffer, width); 8645119bdb952025a30f115b9c6a187173956e55097reed@android.com proc(dst, buffer, width, 0xFF, x, y); 8655119bdb952025a30f115b9c6a187173956e55097reed@android.com y += 1; 8665119bdb952025a30f115b9c6a187173956e55097reed@android.com dst = (uint16_t*)((char*)dst + dstRB); 8675119bdb952025a30f115b9c6a187173956e55097reed@android.com } while (--height); 8685119bdb952025a30f115b9c6a187173956e55097reed@android.com } 8695119bdb952025a30f115b9c6a187173956e55097reed@android.com} 8705119bdb952025a30f115b9c6a187173956e55097reed@android.com 8718a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comstatic inline int count_nonzero_span(const int16_t runs[], const SkAlpha aa[]) { 8728a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int count = 0; 8738a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com for (;;) { 8748a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int n = *runs; 8758a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (n == 0 || *aa == 0) { 8768a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com break; 8778a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 8788a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com runs += n; 8798a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com aa += n; 8808a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com count += n; 8818a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 8828a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com return count; 8838a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 8848a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 8858a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comvoid SkRGB16_Shader_Blitter::blitAntiH(int x, int y, 8868a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com const SkAlpha* SK_RESTRICT antialias, 887a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com const int16_t* SK_RESTRICT runs) { 88887fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkShader::Context* shaderContext = fShaderContext; 8898a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkPMColor* SK_RESTRICT span = fBuffer; 89087fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org uint16_t* SK_RESTRICT device = fDevice.getAddr16(x, y); 8918a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 8928a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com for (;;) { 8938a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int count = *runs; 8948a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (count <= 0) { 8958a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com break; 8968a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 8978a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int aa = *antialias; 8988a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (0 == aa) { 8998a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com device += count; 9008a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com runs += count; 9018a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com antialias += count; 9028a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com x += count; 9038a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com continue; 9048a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 9058a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9068a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int nonZeroCount = count + count_nonzero_span(runs + count, antialias + count); 9078a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9088a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(nonZeroCount <= fDevice.width()); // don't overrun fBuffer 90987fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org shaderContext->shadeSpan(x, y, span, nonZeroCount); 9108a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9118a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkPMColor* localSpan = span; 9128a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com for (;;) { 9138a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkBlitRow::Proc proc = (aa == 0xFF) ? fOpaqueProc : fAlphaProc; 9148a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com proc(device, localSpan, count, aa, x, y); 9158a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9168a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com x += count; 9178a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com device += count; 9188a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com runs += count; 9198a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com antialias += count; 9208a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com nonZeroCount -= count; 9218a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (nonZeroCount == 0) { 9228a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com break; 9238a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 9248a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com localSpan += count; 9258a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(nonZeroCount > 0); 9268a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com count = *runs; 9278a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(count > 0); 9288a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com aa = *antialias; 9298a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 9308a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 9318a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 9328a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9338a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com/////////////////////////////////////////////////////////////////////// 9348a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9358a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comSkRGB16_Shader_Xfermode_Blitter::SkRGB16_Shader_Xfermode_Blitter( 93687fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org const SkBitmap& device, const SkPaint& paint, 93787fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkShader::Context* shaderContext) 93887fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org: INHERITED(device, paint, shaderContext) { 9398a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com fXfermode = paint.getXfermode(); 9408a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(fXfermode); 9418a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com fXfermode->ref(); 9428a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9438a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int width = device.width(); 9448a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com fBuffer = (SkPMColor*)sk_malloc_throw((width + (SkAlign4(width) >> 2)) * sizeof(SkPMColor)); 9458a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com fAAExpand = (uint8_t*)(fBuffer + width); 9468a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 9478a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9488a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comSkRGB16_Shader_Xfermode_Blitter::~SkRGB16_Shader_Xfermode_Blitter() { 9498a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com fXfermode->unref(); 9508a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com sk_free(fBuffer); 9518a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 9528a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9538a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comvoid SkRGB16_Shader_Xfermode_Blitter::blitH(int x, int y, int width) { 9548a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(x + width <= fDevice.width()); 9558a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9568a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com uint16_t* device = fDevice.getAddr16(x, y); 9578a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkPMColor* span = fBuffer; 9588a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 95987fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org fShaderContext->shadeSpan(x, y, span, width); 9608a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com fXfermode->xfer16(device, span, width, NULL); 9618a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 9628a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9638a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.comvoid SkRGB16_Shader_Xfermode_Blitter::blitAntiH(int x, int y, 9648a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com const SkAlpha* SK_RESTRICT antialias, 965a87cd2af4c7f46ba8437c2e500805c9deb9e3a40tomhudson@google.com const int16_t* SK_RESTRICT runs) { 96687fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkShader::Context* shaderContext = fShaderContext; 96787fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkXfermode* mode = fXfermode; 9688a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkPMColor* SK_RESTRICT span = fBuffer; 96987fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org uint8_t* SK_RESTRICT aaExpand = fAAExpand; 97087fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org uint16_t* SK_RESTRICT device = fDevice.getAddr16(x, y); 9718a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9728a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com for (;;) { 9738a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int count = *runs; 9748a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (count <= 0) { 9758a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com break; 9768a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 9778a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int aa = *antialias; 9788a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (0 == aa) { 9798a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com device += count; 9808a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com runs += count; 9818a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com antialias += count; 9828a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com x += count; 9838a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com continue; 9848a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 9858a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9868a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com int nonZeroCount = count + count_nonzero_span(runs + count, 9878a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com antialias + count); 9888a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9898a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(nonZeroCount <= fDevice.width()); // don't overrun fBuffer 99087fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org shaderContext->shadeSpan(x, y, span, nonZeroCount); 9918a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 9928a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com x += nonZeroCount; 9938a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkPMColor* localSpan = span; 9948a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com for (;;) { 9958a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (aa == 0xFF) { 9968a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com mode->xfer16(device, localSpan, count, NULL); 9978a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } else { 9988a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(aa); 9998a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com memset(aaExpand, aa, count); 10008a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com mode->xfer16(device, localSpan, count, aaExpand); 10018a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 10028a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com device += count; 10038a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com runs += count; 10048a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com antialias += count; 10058a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com nonZeroCount -= count; 10068a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com if (nonZeroCount == 0) { 10078a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com break; 10088a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 10098a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com localSpan += count; 10108a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(nonZeroCount > 0); 10118a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com count = *runs; 10128a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com SkASSERT(count > 0); 10138a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com aa = *antialias; 10148a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com } 1015fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com } 10168a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 10178a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 10181fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com/////////////////////////////////////////////////////////////////////////////// 10198a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com 10201fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.comSkBlitter* SkBlitter_ChooseD565(const SkBitmap& device, const SkPaint& paint, 102187fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkShader::Context* shaderContext, 1022a5572e5bb2a2bbeeb59de0741c2527869d365a0ccommit-bot@chromium.org SkTBlitterAllocator* allocator) { 1023a5572e5bb2a2bbeeb59de0741c2527869d365a0ccommit-bot@chromium.org SkASSERT(allocator != NULL); 1024a5572e5bb2a2bbeeb59de0741c2527869d365a0ccommit-bot@chromium.org 10251fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkBlitter* blitter; 10261fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkShader* shader = paint.getShader(); 10271fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkXfermode* mode = paint.getXfermode(); 10281fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com 10291fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com // we require a shader if there is an xfermode, handled by our caller 10301fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkASSERT(NULL == mode || NULL != shader); 10311fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com 10321fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com if (shader) { 103387fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org SkASSERT(shaderContext != NULL); 10341fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com if (mode) { 103587fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org blitter = allocator->createT<SkRGB16_Shader_Xfermode_Blitter>(device, paint, 103687fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org shaderContext); 103787fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org } else if (shaderContext->canCallShadeSpan16()) { 103887fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org blitter = allocator->createT<SkRGB16_Shader16_Blitter>(device, paint, shaderContext); 10391fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com } else { 104087fcd950198a16211b3988610beebb5ca5bcf323commit-bot@chromium.org blitter = allocator->createT<SkRGB16_Shader_Blitter>(device, paint, shaderContext); 10411fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com } 10421fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com } else { 10431fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com // no shader, no xfermode, (and we always ignore colorfilter) 10441fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com SkColor color = paint.getColor(); 10451fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com if (0 == SkColorGetA(color)) { 1046a5572e5bb2a2bbeeb59de0741c2527869d365a0ccommit-bot@chromium.org blitter = allocator->createT<SkNullBlitter>(); 1047867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com#ifdef USE_BLACK_BLITTER 10481fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com } else if (SK_ColorBLACK == color) { 1049a5572e5bb2a2bbeeb59de0741c2527869d365a0ccommit-bot@chromium.org blitter = allocator->createT<SkRGB16_Black_Blitter>(device, paint); 1050867ee807cc95c77aff830e9e6c1988bfbe604405reed@android.com#endif 10511fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com } else if (0xFF == SkColorGetA(color)) { 1052a5572e5bb2a2bbeeb59de0741c2527869d365a0ccommit-bot@chromium.org blitter = allocator->createT<SkRGB16_Opaque_Blitter>(device, paint); 10531fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com } else { 1054a5572e5bb2a2bbeeb59de0741c2527869d365a0ccommit-bot@chromium.org blitter = allocator->createT<SkRGB16_Blitter>(device, paint); 10551fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com } 10561fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com } 1057fbfcd5602128ec010c82cb733c9cdc0a3254f9f3rmistry@google.com 10581fc4c605def61d9e10489f9cd63dc378baa6ade3reed@android.com return blitter; 10598a1c16ff38322f0210116fa7293eb8817c7e477ereed@android.com} 1060