| Index: src/opts/SkBlurImageFilter_opts.h
|
| diff --git a/src/opts/SkBlurImageFilter_opts.h b/src/opts/SkBlurImageFilter_opts.h
|
| index 31d9d5fdbc166e5fedab16638f6c353ed8608969..7844e9fb472ba7f52f0b43a8e0ceadf71ec80427 100644
|
| --- a/src/opts/SkBlurImageFilter_opts.h
|
| +++ b/src/opts/SkBlurImageFilter_opts.h
|
| @@ -16,94 +16,54 @@ namespace SK_OPTS_NS {
|
| enum class BlurDirection { kX, kY };
|
|
|
| #if SK_CPU_SSE_LEVEL >= SK_CPU_SSE_LEVEL_SSE2
|
| -template<BlurDirection srcDirection, BlurDirection dstDirection>
|
| -void box_blur(const SkPMColor* src, int srcStride, SkPMColor* dst, int kernelSize,
|
| - int leftOffset, int rightOffset, int width, int height) {
|
| #if SK_CPU_SSE_LEVEL >= SK_CPU_SSE_LEVEL_SSE41
|
| - // ARGB -> 000A 000R 000G 000B
|
| - auto expand = [](int p) {
|
| - return _mm_cvtepu8_epi32(_mm_cvtsi32_si128(p));
|
| - };
|
| - // Axxx Rxxx Gxxx Bxxx -> ARGB
|
| - auto repack = [](__m128i p) {
|
| - const char _ = ~0; // Don't care what ends up in these bytes. This zeros them.
|
| - p = _mm_shuffle_epi8(p, _mm_set_epi8(_,_,_,_, _,_,_,_, _,_,_,_, 15,11,7,3));
|
| - return _mm_cvtsi128_si32(p);
|
| - };
|
| +// ARGB -> 000A 000R 000G 000B
|
| +static inline __m128i expand(SkPMColor p) {
|
| + return _mm_cvtepu8_epi32(_mm_cvtsi32_si128(p));
|
| +};
|
| +// Axxx Rxxx Gxxx Bxxx -> ARGB
|
| +static inline SkPMColor repack(__m128i p) {
|
| + const char _ = ~0; // Don't care what ends up in these bytes. This zeros them.
|
| + p = _mm_shuffle_epi8(p, _mm_set_epi8(_,_,_,_, _,_,_,_, _,_,_,_, 15,11,7,3));
|
| + return _mm_cvtsi128_si32(p);
|
| +};
|
| +#define mullo_epi32 _mm_mullo_epi32
|
|
|
| #else
|
| - // ARGB -> 000A 000R 000G 000B
|
| - auto expand = [](int p) {
|
| - auto result = _mm_cvtsi32_si128(p);
|
| - result = _mm_unpacklo_epi8(result, _mm_setzero_si128());
|
| - result = _mm_unpacklo_epi16(result, _mm_setzero_si128());
|
| - return result;
|
| - };
|
| - // Axxx Rxxx Gxxx Bxxx -> ARGB
|
| - auto repack = [](__m128i p) {
|
| - p = _mm_srli_epi32(p, 24); // 000A 000R 000G 000B
|
| - p = _mm_packs_epi32(p, p); // xxxx xxxx 0A0R 0G0B
|
| - p = _mm_packus_epi16(p, p); // xxxx xxxx xxxx ARGB
|
| - return _mm_cvtsi128_si32(p);
|
| - };
|
| -
|
| - // _mm_mullo_epi32 is not available, so use the standard trick to emulate it.
|
| - auto _mm_mullo_epi32 = [](__m128i a, __m128i b) {
|
| - __m128i p02 = _mm_mul_epu32(a, b),
|
| - p13 = _mm_mul_epu32(_mm_srli_si128(a, 4),
|
| - _mm_srli_si128(b, 4));
|
| - return _mm_unpacklo_epi32(_mm_shuffle_epi32(p02, _MM_SHUFFLE(0,0,2,0)),
|
| - _mm_shuffle_epi32(p13, _MM_SHUFFLE(0,0,2,0)));
|
| - };
|
| +// ARGB -> 000A 000R 000G 000B
|
| +static inline __m128i expand(int p) {
|
| + auto result = _mm_cvtsi32_si128(p);
|
| + result = _mm_unpacklo_epi8(result, _mm_setzero_si128());
|
| + result = _mm_unpacklo_epi16(result, _mm_setzero_si128());
|
| + return result;
|
| +};
|
| +// Axxx Rxxx Gxxx Bxxx -> ARGB
|
| +static inline SkPMColor repack(__m128i p) {
|
| + p = _mm_srli_epi32(p, 24); // 000A 000R 000G 000B
|
| + p = _mm_packs_epi32(p, p); // xxxx xxxx 0A0R 0G0B
|
| + p = _mm_packus_epi16(p, p); // xxxx xxxx xxxx ARGB
|
| + return _mm_cvtsi128_si32(p);
|
| +};
|
| +
|
| +// _mm_mullo_epi32 is not available, so use the standard trick to emulate it.
|
| +static inline __m128i mullo_epi32(__m128i a, __m128i b) {
|
| + __m128i p02 = _mm_mul_epu32(a, b),
|
| + p13 = _mm_mul_epu32(_mm_srli_si128(a, 4),
|
| + _mm_srli_si128(b, 4));
|
| + return _mm_unpacklo_epi32(_mm_shuffle_epi32(p02, _MM_SHUFFLE(0,0,2,0)),
|
| + _mm_shuffle_epi32(p13, _MM_SHUFFLE(0,0,2,0)));
|
| +};
|
| #endif
|
| - const int rightBorder = SkMin32(rightOffset + 1, width);
|
| - const int srcStrideX = srcDirection == BlurDirection::kX ? 1 : srcStride;
|
| - const int dstStrideX = dstDirection == BlurDirection::kX ? 1 : height;
|
| - const int srcStrideY = srcDirection == BlurDirection::kX ? srcStride : 1;
|
| - const int dstStrideY = dstDirection == BlurDirection::kX ? width : 1;
|
| - const __m128i scale = _mm_set1_epi32((1 << 24) / kernelSize);
|
| - const __m128i half = _mm_set1_epi32(1 << 23);
|
| - for (int y = 0; y < height; ++y) {
|
| - __m128i sum = _mm_setzero_si128();
|
| - const SkPMColor* p = src;
|
| - for (int i = 0; i < rightBorder; ++i) {
|
| - sum = _mm_add_epi32(sum, expand(*p));
|
| - p += srcStrideX;
|
| - }
|
| -
|
| - const SkPMColor* sptr = src;
|
| - SkColor* dptr = dst;
|
| - for (int x = 0; x < width; ++x) {
|
| - // TODO(mtklein): We are working in 8.24 here. Drop to 8.8 when the kernel is narrow?
|
| - // Multiply each component by scale (divide by kernel size) and add half to round.
|
| - auto result = _mm_mullo_epi32(sum, scale);
|
| - result = _mm_add_epi32(result, half);
|
| -
|
| - // Now pack the top byte of each 32-bit lane back down into one 32-bit color.
|
| - // Axxx Rxxx Gxxx Bxxx -> xxxx xxxx xxxx ARGB
|
| - *dptr = repack(result);
|
| -
|
| - // TODO(mtklein): experiment with breaking this loop into 3 parts
|
| - if (x >= leftOffset) {
|
| - SkColor l = *(sptr - leftOffset * srcStrideX);
|
| - sum = _mm_sub_epi32(sum, expand(l));
|
| - }
|
| - if (x + rightOffset + 1 < width) {
|
| - SkColor r = *(sptr + (rightOffset + 1) * srcStrideX);
|
| - sum = _mm_add_epi32(sum, expand(r));
|
| - }
|
| - sptr += srcStrideX;
|
| - if (srcDirection == BlurDirection::kY) {
|
| - // TODO(mtklein): experiment with moving this prefetch forward
|
| - _mm_prefetch(reinterpret_cast<const char*>(sptr + (rightOffset + 1) * srcStrideX),
|
| - _MM_HINT_T0);
|
| - }
|
| - dptr += dstStrideX;
|
| - }
|
| - src += srcStrideY;
|
| - dst += dstStrideY;
|
| - }
|
| -}
|
| +#define INIT_SCALE const __m128i scale = _mm_set1_epi32((1 << 24) / kernelSize);
|
| +#define INIT_HALF const __m128i half = _mm_set1_epi32(1 << 23);
|
| +#define INIT_SUMS __m128i sum = _mm_setzero_si128();
|
| +#define INCREMENT_SUMS(c) sum = _mm_add_epi32(sum, expand(c))
|
| +#define DECREMENT_SUMS(c) sum = _mm_sub_epi32(sum, expand(c))
|
| +#define STORE_SUMS \
|
| + auto result = mullo_epi32(sum, scale); \
|
| + result = _mm_add_epi32(result, half); \
|
| + *dptr = repack(result);
|
| +#define DOUBLE_ROW_OPTIMIZATION
|
|
|
| #elif defined(SK_ARM_HAS_NEON)
|
|
|
| @@ -167,72 +127,52 @@ void box_blur_double(const SkPMColor** src, int srcStride, SkPMColor** dst, int
|
| }
|
| }
|
|
|
| -template<BlurDirection srcDirection, BlurDirection dstDirection>
|
| -void box_blur(const SkPMColor* src, int srcStride, SkPMColor* dst, int kernelSize,
|
| - int leftOffset, int rightOffset, int width, int height) {
|
| - // ARGB -> 0A0R 0G0B
|
| - auto expand = [](uint32_t p) {
|
| - return vget_low_u16(vmovl_u8(vreinterpret_u8_u32(vdup_n_u32(p))));
|
| - };
|
| - const int rightBorder = SkMin32(rightOffset + 1, width);
|
| - const int srcStrideX = srcDirection == BlurDirection::kX ? 1 : srcStride;
|
| - const int dstStrideX = dstDirection == BlurDirection::kX ? 1 : height;
|
| - const int srcStrideY = srcDirection == BlurDirection::kX ? srcStride : 1;
|
| - const int dstStrideY = dstDirection == BlurDirection::kX ? width : 1;
|
| - const uint32x4_t scale = vdupq_n_u32((1 << 24) / kernelSize);
|
| - const uint32x4_t half = vdupq_n_u32(1 << 23);
|
| -
|
| - if (1 < kernelSize && kernelSize < 128) {
|
| - box_blur_double<srcDirection, dstDirection>(&src, srcStride, &dst, kernelSize,
|
| - leftOffset, rightOffset, width, &height);
|
| +// ARGB -> 0A0R 0G0B
|
| +static inline uint16x4_t expand(SkPMColor p) {
|
| + return vget_low_u16(vmovl_u8(vreinterpret_u8_u32(vdup_n_u32(p))));
|
| +};
|
| +
|
| +#define INIT_SCALE const uint32x4_t scale = vdupq_n_u32((1 << 24) / kernelSize);
|
| +#define INIT_HALF const uint32x4_t half = vdupq_n_u32(1 << 23);
|
| +#define INIT_SUMS uint32x4_t sum = vdupq_n_u32(0);
|
| +#define INCREMENT_SUMS(c) sum = vaddw_u16(sum, expand(c));
|
| +#define DECREMENT_SUMS(c) sum = vsubw_u16(sum, expand(c));
|
| +
|
| +#define STORE_SUMS \
|
| + uint32x4_t result = vmlaq_u32(half, sum, scale); \
|
| + uint16x4_t result16 = vqshrn_n_u32(result, 16); \
|
| + uint8x8_t result8 = vqshrn_n_u16(vcombine_u16(result16, result16), 8); \
|
| + vst1_lane_u32(dptr, vreinterpret_u32_u8(result8), 0);
|
| +
|
| +#define DOUBLE_ROW_OPTIMIZATION \
|
| + if (1 < kernelSize && kernelSize < 128) { \
|
| + box_blur_double<srcDirection, dstDirection>(&src, srcStride, &dst, kernelSize, \
|
| + leftOffset, rightOffset, width, &height); \
|
| }
|
|
|
| - for (; height > 0; height--) {
|
| - uint32x4_t sum = vdupq_n_u32(0);
|
| - const SkPMColor* p = src;
|
| - for (int i = 0; i < rightBorder; ++i) {
|
| - sum = vaddw_u16(sum, expand(*p));
|
| - p += srcStrideX;
|
| - }
|
| -
|
| - const SkPMColor* sptr = src;
|
| - SkPMColor* dptr = dst;
|
| - for (int x = 0; x < width; ++x) {
|
| - // ( half+sumA*scale half+sumR*scale half+sumG*scale half+sumB*scale )
|
| - uint32x4_t result = vmlaq_u32(half, sum, scale);
|
| -
|
| - // Saturated conversion to 16-bit.
|
| - // ( AAAA RRRR GGGG BBBB ) -> ( 0A 0R 0G 0B )
|
| - uint16x4_t result16 = vqshrn_n_u32(result, 16);
|
| -
|
| - // Saturated conversion to 8-bit.
|
| - // ( 0A 0R 0G 0B ) -> ( 0A 0R 0G 0B 0A 0R 0G 0B ) -> ( A R G B A R G B )
|
| - uint8x8_t result8 = vqshrn_n_u16(vcombine_u16(result16, result16), 8);
|
| -
|
| - // ( A R G B A R G B ) -> ( ARGB ARGB ) -> ( ARGB )
|
| - // Store low 32 bits to destination.
|
| - vst1_lane_u32(dptr, vreinterpret_u32_u8(result8), 0);
|
| +#else // Neither NEON nor >=SSE2.
|
|
|
| - if (x >= leftOffset) {
|
| - const SkPMColor* l = sptr - leftOffset * srcStrideX;
|
| - sum = vsubw_u16(sum, expand(*l));
|
| - }
|
| - if (x + rightOffset + 1 < width) {
|
| - const SkPMColor* r = sptr + (rightOffset + 1) * srcStrideX;
|
| - sum = vaddw_u16(sum, expand(*r));
|
| - }
|
| - sptr += srcStrideX;
|
| - if (srcDirection == BlurDirection::kX) {
|
| - SK_PREFETCH(sptr + (rightOffset + 16) * srcStrideX);
|
| - }
|
| - dptr += dstStrideX;
|
| - }
|
| - src += srcStrideY;
|
| - dst += dstStrideY;
|
| - }
|
| -}
|
| +#define INIT_SCALE uint32_t scale = (1 << 24) / kernelSize;
|
| +#define INIT_HALF uint32_t half = 1 << 23;
|
| +#define INIT_SUMS int sumA = 0, sumR = 0, sumG = 0, sumB = 0;
|
| +#define INCREMENT_SUMS(c) \
|
| + sumA += SkGetPackedA32(c); \
|
| + sumR += SkGetPackedR32(c); \
|
| + sumG += SkGetPackedG32(c); \
|
| + sumB += SkGetPackedB32(c)
|
| +#define DECREMENT_SUMS(c) \
|
| + sumA -= SkGetPackedA32(c); \
|
| + sumR -= SkGetPackedR32(c); \
|
| + sumG -= SkGetPackedG32(c); \
|
| + sumB -= SkGetPackedB32(c)
|
| +#define STORE_SUMS \
|
| + *dptr = SkPackARGB32((sumA * scale + half) >> 24, \
|
| + (sumR * scale + half) >> 24, \
|
| + (sumG * scale + half) >> 24, \
|
| + (sumB * scale + half) >> 24);
|
| +#define DOUBLE_ROW_OPTIMIZATION
|
|
|
| -#else // Neither NEON nor >=SSE2.
|
| +#endif
|
|
|
| template<BlurDirection srcDirection, BlurDirection dstDirection>
|
| static void box_blur(const SkPMColor* src, int srcStride, SkPMColor* dst, int kernelSize,
|
| @@ -242,43 +182,34 @@ static void box_blur(const SkPMColor* src, int srcStride, SkPMColor* dst, int ke
|
| int dstStrideX = dstDirection == BlurDirection::kX ? 1 : height;
|
| int srcStrideY = srcDirection == BlurDirection::kX ? srcStride : 1;
|
| int dstStrideY = dstDirection == BlurDirection::kX ? width : 1;
|
| - uint32_t scale = (1 << 24) / kernelSize;
|
| - uint32_t half = 1 << 23;
|
| + INIT_SCALE
|
| + INIT_HALF
|
| +
|
| + DOUBLE_ROW_OPTIMIZATION
|
| +
|
| for (int y = 0; y < height; ++y) {
|
| - int sumA = 0, sumR = 0, sumG = 0, sumB = 0;
|
| + INIT_SUMS
|
| const SkPMColor* p = src;
|
| for (int i = 0; i < rightBorder; ++i) {
|
| - sumA += SkGetPackedA32(*p);
|
| - sumR += SkGetPackedR32(*p);
|
| - sumG += SkGetPackedG32(*p);
|
| - sumB += SkGetPackedB32(*p);
|
| + INCREMENT_SUMS(*p);
|
| p += srcStrideX;
|
| }
|
|
|
| const SkPMColor* sptr = src;
|
| SkColor* dptr = dst;
|
| for (int x = 0; x < width; ++x) {
|
| - *dptr = SkPackARGB32((sumA * scale + half) >> 24,
|
| - (sumR * scale + half) >> 24,
|
| - (sumG * scale + half) >> 24,
|
| - (sumB * scale + half) >> 24);
|
| + STORE_SUMS
|
| if (x >= leftOffset) {
|
| SkColor l = *(sptr - leftOffset * srcStrideX);
|
| - sumA -= SkGetPackedA32(l);
|
| - sumR -= SkGetPackedR32(l);
|
| - sumG -= SkGetPackedG32(l);
|
| - sumB -= SkGetPackedB32(l);
|
| + DECREMENT_SUMS(l);
|
| }
|
| if (x + rightOffset + 1 < width) {
|
| SkColor r = *(sptr + (rightOffset + 1) * srcStrideX);
|
| - sumA += SkGetPackedA32(r);
|
| - sumR += SkGetPackedR32(r);
|
| - sumG += SkGetPackedG32(r);
|
| - sumB += SkGetPackedB32(r);
|
| + INCREMENT_SUMS(r);
|
| }
|
| sptr += srcStrideX;
|
| if (srcDirection == BlurDirection::kY) {
|
| - SK_PREFETCH(sptr + (rightOffset + 1) * srcStrideX);
|
| + SK_PREFETCH(reinterpret_cast<const char*>(sptr + (rightOffset + 1) * srcStrideX));
|
| }
|
| dptr += dstStrideX;
|
| }
|
| @@ -287,8 +218,6 @@ static void box_blur(const SkPMColor* src, int srcStride, SkPMColor* dst, int ke
|
| }
|
| }
|
|
|
| -#endif
|
| -
|
| static auto box_blur_xx = &box_blur<BlurDirection::kX, BlurDirection::kX>,
|
| box_blur_xy = &box_blur<BlurDirection::kX, BlurDirection::kY>,
|
| box_blur_yx = &box_blur<BlurDirection::kY, BlurDirection::kX>;
|
|
|