From 30f41c02aec763d32e62351452da9ef582bc3472 Mon Sep 17 00:00:00 2001 From: 3gg <3gg@shellblade.net> Date: Fri, 6 Mar 2026 13:30:59 -0800 Subject: Move contrib libraries to contrib repo --- contrib/SDL-3.2.8/src/video/SDL_blit_A.c | 1461 ------------------------------ 1 file changed, 1461 deletions(-) delete mode 100644 contrib/SDL-3.2.8/src/video/SDL_blit_A.c (limited to 'contrib/SDL-3.2.8/src/video/SDL_blit_A.c') diff --git a/contrib/SDL-3.2.8/src/video/SDL_blit_A.c b/contrib/SDL-3.2.8/src/video/SDL_blit_A.c deleted file mode 100644 index 5d6d92d..0000000 --- a/contrib/SDL-3.2.8/src/video/SDL_blit_A.c +++ /dev/null @@ -1,1461 +0,0 @@ -/* - Simple DirectMedia Layer - Copyright (C) 1997-2025 Sam Lantinga - - This software is provided 'as-is', without any express or implied - warranty. In no event will the authors be held liable for any damages - arising from the use of this software. - - Permission is granted to anyone to use this software for any purpose, - including commercial applications, and to alter it and redistribute it - freely, subject to the following restrictions: - - 1. The origin of this software must not be misrepresented; you must not - claim that you wrote the original software. If you use this software - in a product, an acknowledgment in the product documentation would be - appreciated but is not required. - 2. Altered source versions must be plainly marked as such, and must not be - misrepresented as being the original software. - 3. This notice may not be removed or altered from any source distribution. -*/ -#include "SDL_internal.h" - -#ifdef SDL_HAVE_BLIT_A - -#include "SDL_surface_c.h" - -// Functions to perform alpha blended blitting - -// N->1 blending with per-surface alpha -static void BlitNto1SurfaceAlpha(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint8 *src = info->src; - int srcskip = info->src_skip; - Uint8 *dst = info->dst; - int dstskip = info->dst_skip; - Uint8 *palmap = info->table; - const SDL_PixelFormatDetails *srcfmt = info->src_fmt; - const SDL_Color *dstpal = info->dst_pal->colors; - int srcbpp = srcfmt->bytes_per_pixel; - Uint32 Pixel; - unsigned sR, sG, sB; - unsigned dR, dG, dB; - const unsigned A = info->a; - - while (height--) { - /* *INDENT-OFF* */ // clang-format off - DUFFS_LOOP( - { - DISEMBLE_RGB(src, srcbpp, srcfmt, Pixel, sR, sG, sB); - dR = dstpal[*dst].r; - dG = dstpal[*dst].g; - dB = dstpal[*dst].b; - ALPHA_BLEND_RGB(sR, sG, sB, A, dR, dG, dB); - dR &= 0xff; - dG &= 0xff; - dB &= 0xff; - // Pack RGB into 8bit pixel - if ( palmap == NULL ) { - *dst = (Uint8)(((dR>>5)<<(3+2))|((dG>>5)<<(2))|((dB>>6)<<(0))); - } else { - *dst = palmap[((dR>>5)<<(3+2))|((dG>>5)<<(2))|((dB>>6)<<(0))]; - } - dst++; - src += srcbpp; - }, - width); - /* *INDENT-ON* */ // clang-format on - src += srcskip; - dst += dstskip; - } -} - -// N->1 blending with pixel alpha -static void BlitNto1PixelAlpha(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint8 *src = info->src; - int srcskip = info->src_skip; - Uint8 *dst = info->dst; - int dstskip = info->dst_skip; - Uint8 *palmap = info->table; - const SDL_PixelFormatDetails *srcfmt = info->src_fmt; - const SDL_Color *dstpal = info->dst_pal->colors; - int srcbpp = srcfmt->bytes_per_pixel; - Uint32 Pixel; - unsigned sR, sG, sB, sA; - unsigned dR, dG, dB; - - while (height--) { - /* *INDENT-OFF* */ // clang-format off - DUFFS_LOOP( - { - DISEMBLE_RGBA(src,srcbpp,srcfmt,Pixel,sR,sG,sB,sA); - dR = dstpal[*dst].r; - dG = dstpal[*dst].g; - dB = dstpal[*dst].b; - ALPHA_BLEND_RGB(sR, sG, sB, sA, dR, dG, dB); - dR &= 0xff; - dG &= 0xff; - dB &= 0xff; - // Pack RGB into 8bit pixel - if ( palmap == NULL ) { - *dst = (Uint8)(((dR>>5)<<(3+2))|((dG>>5)<<(2))|((dB>>6)<<(0))); - } else { - *dst = palmap[((dR>>5)<<(3+2))|((dG>>5)<<(2))|((dB>>6)<<(0))]; - } - dst++; - src += srcbpp; - }, - width); - /* *INDENT-ON* */ // clang-format on - src += srcskip; - dst += dstskip; - } -} - -// colorkeyed N->1 blending with per-surface alpha -static void BlitNto1SurfaceAlphaKey(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint8 *src = info->src; - int srcskip = info->src_skip; - Uint8 *dst = info->dst; - int dstskip = info->dst_skip; - Uint8 *palmap = info->table; - const SDL_PixelFormatDetails *srcfmt = info->src_fmt; - const SDL_Color *dstpal = info->dst_pal->colors; - int srcbpp = srcfmt->bytes_per_pixel; - Uint32 ckey = info->colorkey; - Uint32 Pixel; - unsigned sR, sG, sB; - unsigned dR, dG, dB; - const unsigned A = info->a; - - while (height--) { - /* *INDENT-OFF* */ // clang-format off - DUFFS_LOOP( - { - DISEMBLE_RGB(src, srcbpp, srcfmt, Pixel, sR, sG, sB); - if ( Pixel != ckey ) { - dR = dstpal[*dst].r; - dG = dstpal[*dst].g; - dB = dstpal[*dst].b; - ALPHA_BLEND_RGB(sR, sG, sB, A, dR, dG, dB); - dR &= 0xff; - dG &= 0xff; - dB &= 0xff; - // Pack RGB into 8bit pixel - if ( palmap == NULL ) { - *dst = (Uint8)(((dR>>5)<<(3+2))|((dG>>5)<<(2))|((dB>>6)<<(0))); - } else { - *dst = palmap[((dR>>5)<<(3+2))|((dG>>5)<<(2))|((dB>>6)<<(0))]; - } - } - dst++; - src += srcbpp; - }, - width); - /* *INDENT-ON* */ // clang-format on - src += srcskip; - dst += dstskip; - } -} - -#ifdef SDL_SSE2_INTRINSICS - -static void SDL_TARGETING("sse2") Blit888to888SurfaceAlphaSSE2(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint8 *src = info->src; - int srcskip = info->src_skip; - Uint8 *dst = info->dst; - int dstskip = info->dst_skip; - Uint8 alpha = info->a; - - const __m128i alpha_fill_mask = _mm_set1_epi32((int)0xff000000); - const __m128i srcA = _mm_set1_epi16(alpha); - - while (height--) { - int i = 0; - - for (; i + 4 <= width; i += 4) { - // Load 4 src pixels - __m128i src128 = _mm_loadu_si128((__m128i *)src); - - // Load 4 dst pixels - __m128i dst128 = _mm_loadu_si128((__m128i *)dst); - - __m128i src_lo = _mm_unpacklo_epi8(src128, _mm_setzero_si128()); - __m128i src_hi = _mm_unpackhi_epi8(src128, _mm_setzero_si128()); - - __m128i dst_lo = _mm_unpacklo_epi8(dst128, _mm_setzero_si128()); - __m128i dst_hi = _mm_unpackhi_epi8(dst128, _mm_setzero_si128()); - - // dst = ((src - dst) * srcA) + ((dst << 8) - dst) - dst_lo = _mm_add_epi16(_mm_mullo_epi16(_mm_sub_epi16(src_lo, dst_lo), srcA), - _mm_sub_epi16(_mm_slli_epi16(dst_lo, 8), dst_lo)); - dst_hi = _mm_add_epi16(_mm_mullo_epi16(_mm_sub_epi16(src_hi, dst_hi), srcA), - _mm_sub_epi16(_mm_slli_epi16(dst_hi, 8), dst_hi)); - - // dst += 0x1U (use 0x80 to round instead of floor) - dst_lo = _mm_add_epi16(dst_lo, _mm_set1_epi16(1)); - dst_hi = _mm_add_epi16(dst_hi, _mm_set1_epi16(1)); - - // dst = (dst + (dst >> 8)) >> 8 - dst_lo = _mm_srli_epi16(_mm_add_epi16(dst_lo, _mm_srli_epi16(dst_lo, 8)), 8); - dst_hi = _mm_srli_epi16(_mm_add_epi16(dst_hi, _mm_srli_epi16(dst_hi, 8)), 8); - - dst128 = _mm_packus_epi16(dst_lo, dst_hi); - - // Set the alpha channels of dst to 255 - dst128 = _mm_or_si128(dst128, alpha_fill_mask); - - _mm_storeu_si128((__m128i *)dst, dst128); - - src += 16; - dst += 16; - } - - for (; i < width; ++i) { - Uint32 src32 = *(Uint32 *)src; - Uint32 dst32 = *(Uint32 *)dst; - - FACTOR_BLEND_8888(src32, dst32, alpha); - - *dst = dst32 | 0xff000000; - - src += 4; - dst += 4; - } - - src += srcskip; - dst += dstskip; - } -} - -#endif - -// fast RGB888->(A)RGB888 blending with surface alpha=128 special case -static void BlitRGBtoRGBSurfaceAlpha128(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint32 *srcp = (Uint32 *)info->src; - int srcskip = info->src_skip >> 2; - Uint32 *dstp = (Uint32 *)info->dst; - int dstskip = info->dst_skip >> 2; - - while (height--) { - /* *INDENT-OFF* */ // clang-format off - DUFFS_LOOP({ - Uint32 s = *srcp++; - Uint32 d = *dstp; - *dstp++ = ((((s & 0x00fefefe) + (d & 0x00fefefe)) >> 1) - + (s & d & 0x00010101)) | 0xff000000; - }, width); - /* *INDENT-ON* */ // clang-format on - srcp += srcskip; - dstp += dstskip; - } -} - -// fast RGB888->(A)RGB888 blending with surface alpha -static void BlitRGBtoRGBSurfaceAlpha(SDL_BlitInfo *info) -{ - unsigned alpha = info->a; - if (alpha == 128) { - BlitRGBtoRGBSurfaceAlpha128(info); - } else { - int width = info->dst_w; - int height = info->dst_h; - Uint32 *srcp = (Uint32 *)info->src; - int srcskip = info->src_skip >> 2; - Uint32 *dstp = (Uint32 *)info->dst; - int dstskip = info->dst_skip >> 2; - Uint32 s; - Uint32 d; - - while (height--) { - /* *INDENT-OFF* */ // clang-format off - DUFFS_LOOP({ - s = *srcp; - d = *dstp; - - FACTOR_BLEND_8888(s, d, alpha); - - *dstp = d | 0xff000000; - ++srcp; - ++dstp; - }, width); - /* *INDENT-ON* */ // clang-format on - srcp += srcskip; - dstp += dstskip; - } - } -} - -// 16bpp special case for per-surface alpha=50%: blend 2 pixels in parallel - -// blend a single 16 bit pixel at 50% -#define BLEND16_50(d, s, mask) \ - ((((s & mask) + (d & mask)) >> 1) + (s & d & (~mask & 0xffff))) - -// blend two 16 bit pixels at 50% -#define BLEND2x16_50(d, s, mask) \ - (((s & (mask | mask << 16)) >> 1) + ((d & (mask | mask << 16)) >> 1) + (s & d & (~(mask | mask << 16)))) - -static void Blit16to16SurfaceAlpha128(SDL_BlitInfo *info, Uint16 mask) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint16 *srcp = (Uint16 *)info->src; - int srcskip = info->src_skip >> 1; - Uint16 *dstp = (Uint16 *)info->dst; - int dstskip = info->dst_skip >> 1; - - while (height--) { - if (((uintptr_t)srcp ^ (uintptr_t)dstp) & 2) { - /* - * Source and destination not aligned, pipeline it. - * This is mostly a win for big blits but no loss for - * small ones - */ - Uint32 prev_sw; - int w = width; - - // handle odd destination - if ((uintptr_t)dstp & 2) { - Uint16 d = *dstp, s = *srcp; - *dstp = BLEND16_50(d, s, mask); - dstp++; - srcp++; - w--; - } - srcp++; // srcp is now 32-bit aligned - - // bootstrap pipeline with first halfword - prev_sw = ((Uint32 *)srcp)[-1]; - - while (w > 1) { - Uint32 sw, dw, s; - sw = *(Uint32 *)srcp; - dw = *(Uint32 *)dstp; -#if SDL_BYTEORDER == SDL_BIG_ENDIAN - s = (prev_sw << 16) + (sw >> 16); -#else - s = (prev_sw >> 16) + (sw << 16); -#endif - prev_sw = sw; - *(Uint32 *)dstp = BLEND2x16_50(dw, s, mask); - dstp += 2; - srcp += 2; - w -= 2; - } - - // final pixel if any - if (w) { - Uint16 d = *dstp, s; -#if SDL_BYTEORDER == SDL_BIG_ENDIAN - s = (Uint16)prev_sw; -#else - s = (Uint16)(prev_sw >> 16); -#endif - *dstp = BLEND16_50(d, s, mask); - srcp++; - dstp++; - } - srcp += srcskip - 1; - dstp += dstskip; - } else { - // source and destination are aligned - int w = width; - - // first odd pixel? - if ((uintptr_t)srcp & 2) { - Uint16 d = *dstp, s = *srcp; - *dstp = BLEND16_50(d, s, mask); - srcp++; - dstp++; - w--; - } - // srcp and dstp are now 32-bit aligned - - while (w > 1) { - Uint32 sw = *(Uint32 *)srcp; - Uint32 dw = *(Uint32 *)dstp; - *(Uint32 *)dstp = BLEND2x16_50(dw, sw, mask); - srcp += 2; - dstp += 2; - w -= 2; - } - - // last odd pixel? - if (w) { - Uint16 d = *dstp, s = *srcp; - *dstp = BLEND16_50(d, s, mask); - srcp++; - dstp++; - } - srcp += srcskip; - dstp += dstskip; - } - } -} - -#ifdef SDL_MMX_INTRINSICS - -// fast RGB565->RGB565 blending with surface alpha -static void SDL_TARGETING("mmx") Blit565to565SurfaceAlphaMMX(SDL_BlitInfo *info) -{ - unsigned alpha = info->a; - if (alpha == 128) { - Blit16to16SurfaceAlpha128(info, 0xf7de); - } else { - int width = info->dst_w; - int height = info->dst_h; - Uint16 *srcp = (Uint16 *)info->src; - int srcskip = info->src_skip >> 1; - Uint16 *dstp = (Uint16 *)info->dst; - int dstskip = info->dst_skip >> 1; - Uint32 s, d; - -#ifdef USE_DUFFS_LOOP - __m64 src1, dst1, src2, dst2, gmask, bmask, mm_res, mm_alpha; - - alpha &= ~(1 + 2 + 4); // cut alpha to get the exact same behaviour - mm_alpha = _mm_set_pi32(0, alpha); // 0000000A -> mm_alpha - alpha >>= 3; // downscale alpha to 5 bits - - mm_alpha = _mm_unpacklo_pi16(mm_alpha, mm_alpha); // 00000A0A -> mm_alpha - mm_alpha = _mm_unpacklo_pi32(mm_alpha, mm_alpha); // 0A0A0A0A -> mm_alpha - /* position alpha to allow for mullo and mulhi on diff channels - to reduce the number of operations */ - mm_alpha = _mm_slli_si64(mm_alpha, 3); - - // Setup the 565 color channel masks - gmask = _mm_set_pi32(0x07E007E0, 0x07E007E0); // MASKGREEN -> gmask - bmask = _mm_set_pi32(0x001F001F, 0x001F001F); // MASKBLUE -> bmask -#endif - - while (height--) { - /* *INDENT-OFF* */ // clang-format off - DUFFS_LOOP_124( - { - s = *srcp++; - d = *dstp; - /* - * shift out the middle component (green) to - * the high 16 bits, and process all three RGB - * components at the same time. - */ - s = (s | s << 16) & 0x07e0f81f; - d = (d | d << 16) & 0x07e0f81f; - d += (s - d) * alpha >> 5; - d &= 0x07e0f81f; - *dstp++ = (Uint16)(d | d >> 16); - },{ - s = *srcp++; - d = *dstp; - /* - * shift out the middle component (green) to - * the high 16 bits, and process all three RGB - * components at the same time. - */ - s = (s | s << 16) & 0x07e0f81f; - d = (d | d << 16) & 0x07e0f81f; - d += (s - d) * alpha >> 5; - d &= 0x07e0f81f; - *dstp++ = (Uint16)(d | d >> 16); - s = *srcp++; - d = *dstp; - /* - * shift out the middle component (green) to - * the high 16 bits, and process all three RGB - * components at the same time. - */ - s = (s | s << 16) & 0x07e0f81f; - d = (d | d << 16) & 0x07e0f81f; - d += (s - d) * alpha >> 5; - d &= 0x07e0f81f; - *dstp++ = (Uint16)(d | d >> 16); - },{ - src1 = *(__m64*)srcp; // 4 src pixels -> src1 - dst1 = *(__m64*)dstp; // 4 dst pixels -> dst1 - - // red - src2 = src1; - src2 = _mm_srli_pi16(src2, 11); // src2 >> 11 -> src2 [000r 000r 000r 000r] - - dst2 = dst1; - dst2 = _mm_srli_pi16(dst2, 11); // dst2 >> 11 -> dst2 [000r 000r 000r 000r] - - // blend - src2 = _mm_sub_pi16(src2, dst2);// src - dst -> src2 - src2 = _mm_mullo_pi16(src2, mm_alpha); /* src2 * alpha -> src2 */ - src2 = _mm_srli_pi16(src2, 11); // src2 >> 11 -> src2 - dst2 = _mm_add_pi16(src2, dst2); // src2 + dst2 -> dst2 - dst2 = _mm_slli_pi16(dst2, 11); // dst2 << 11 -> dst2 - - mm_res = dst2; // RED -> mm_res - - // green -- process the bits in place - src2 = src1; - src2 = _mm_and_si64(src2, gmask); // src & MASKGREEN -> src2 - - dst2 = dst1; - dst2 = _mm_and_si64(dst2, gmask); // dst & MASKGREEN -> dst2 - - // blend - src2 = _mm_sub_pi16(src2, dst2);// src - dst -> src2 - src2 = _mm_mulhi_pi16(src2, mm_alpha); /* src2 * alpha -> src2 */ - src2 = _mm_slli_pi16(src2, 5); // src2 << 5 -> src2 - dst2 = _mm_add_pi16(src2, dst2); // src2 + dst2 -> dst2 - - mm_res = _mm_or_si64(mm_res, dst2); // RED | GREEN -> mm_res - - // blue - src2 = src1; - src2 = _mm_and_si64(src2, bmask); // src & MASKBLUE -> src2[000b 000b 000b 000b] - - dst2 = dst1; - dst2 = _mm_and_si64(dst2, bmask); // dst & MASKBLUE -> dst2[000b 000b 000b 000b] - - // blend - src2 = _mm_sub_pi16(src2, dst2);// src - dst -> src2 - src2 = _mm_mullo_pi16(src2, mm_alpha); /* src2 * alpha -> src2 */ - src2 = _mm_srli_pi16(src2, 11); // src2 >> 11 -> src2 - dst2 = _mm_add_pi16(src2, dst2); // src2 + dst2 -> dst2 - dst2 = _mm_and_si64(dst2, bmask); // dst2 & MASKBLUE -> dst2 - - mm_res = _mm_or_si64(mm_res, dst2); // RED | GREEN | BLUE -> mm_res - - *(__m64*)dstp = mm_res; // mm_res -> 4 dst pixels - - srcp += 4; - dstp += 4; - }, width); - /* *INDENT-ON* */ // clang-format on - srcp += srcskip; - dstp += dstskip; - } - _mm_empty(); - } -} - -// fast RGB555->RGB555 blending with surface alpha -static void SDL_TARGETING("mmx") Blit555to555SurfaceAlphaMMX(SDL_BlitInfo *info) -{ - unsigned alpha = info->a; - if (alpha == 128) { - Blit16to16SurfaceAlpha128(info, 0xfbde); - } else { - int width = info->dst_w; - int height = info->dst_h; - Uint16 *srcp = (Uint16 *)info->src; - int srcskip = info->src_skip >> 1; - Uint16 *dstp = (Uint16 *)info->dst; - int dstskip = info->dst_skip >> 1; - Uint32 s, d; - -#ifdef USE_DUFFS_LOOP - __m64 src1, dst1, src2, dst2, rmask, gmask, bmask, mm_res, mm_alpha; - - alpha &= ~(1 + 2 + 4); // cut alpha to get the exact same behaviour - mm_alpha = _mm_set_pi32(0, alpha); // 0000000A -> mm_alpha - alpha >>= 3; // downscale alpha to 5 bits - - mm_alpha = _mm_unpacklo_pi16(mm_alpha, mm_alpha); // 00000A0A -> mm_alpha - mm_alpha = _mm_unpacklo_pi32(mm_alpha, mm_alpha); // 0A0A0A0A -> mm_alpha - /* position alpha to allow for mullo and mulhi on diff channels - to reduce the number of operations */ - mm_alpha = _mm_slli_si64(mm_alpha, 3); - - // Setup the 555 color channel masks - rmask = _mm_set_pi32(0x7C007C00, 0x7C007C00); // MASKRED -> rmask - gmask = _mm_set_pi32(0x03E003E0, 0x03E003E0); // MASKGREEN -> gmask - bmask = _mm_set_pi32(0x001F001F, 0x001F001F); // MASKBLUE -> bmask -#endif - while (height--) { - /* *INDENT-OFF* */ // clang-format off - DUFFS_LOOP_124( - { - s = *srcp++; - d = *dstp; - /* - * shift out the middle component (green) to - * the high 16 bits, and process all three RGB - * components at the same time. - */ - s = (s | s << 16) & 0x03e07c1f; - d = (d | d << 16) & 0x03e07c1f; - d += (s - d) * alpha >> 5; - d &= 0x03e07c1f; - *dstp++ = (Uint16)(d | d >> 16); - },{ - s = *srcp++; - d = *dstp; - /* - * shift out the middle component (green) to - * the high 16 bits, and process all three RGB - * components at the same time. - */ - s = (s | s << 16) & 0x03e07c1f; - d = (d | d << 16) & 0x03e07c1f; - d += (s - d) * alpha >> 5; - d &= 0x03e07c1f; - *dstp++ = (Uint16)(d | d >> 16); - s = *srcp++; - d = *dstp; - /* - * shift out the middle component (green) to - * the high 16 bits, and process all three RGB - * components at the same time. - */ - s = (s | s << 16) & 0x03e07c1f; - d = (d | d << 16) & 0x03e07c1f; - d += (s - d) * alpha >> 5; - d &= 0x03e07c1f; - *dstp++ = (Uint16)(d | d >> 16); - },{ - src1 = *(__m64*)srcp; // 4 src pixels -> src1 - dst1 = *(__m64*)dstp; // 4 dst pixels -> dst1 - - // red -- process the bits in place - src2 = src1; - src2 = _mm_and_si64(src2, rmask); // src & MASKRED -> src2 - - dst2 = dst1; - dst2 = _mm_and_si64(dst2, rmask); // dst & MASKRED -> dst2 - - // blend - src2 = _mm_sub_pi16(src2, dst2);// src - dst -> src2 - src2 = _mm_mulhi_pi16(src2, mm_alpha); /* src2 * alpha -> src2 */ - src2 = _mm_slli_pi16(src2, 5); // src2 << 5 -> src2 - dst2 = _mm_add_pi16(src2, dst2); // src2 + dst2 -> dst2 - dst2 = _mm_and_si64(dst2, rmask); // dst2 & MASKRED -> dst2 - - mm_res = dst2; // RED -> mm_res - - // green -- process the bits in place - src2 = src1; - src2 = _mm_and_si64(src2, gmask); // src & MASKGREEN -> src2 - - dst2 = dst1; - dst2 = _mm_and_si64(dst2, gmask); // dst & MASKGREEN -> dst2 - - // blend - src2 = _mm_sub_pi16(src2, dst2);// src - dst -> src2 - src2 = _mm_mulhi_pi16(src2, mm_alpha); /* src2 * alpha -> src2 */ - src2 = _mm_slli_pi16(src2, 5); // src2 << 5 -> src2 - dst2 = _mm_add_pi16(src2, dst2); // src2 + dst2 -> dst2 - - mm_res = _mm_or_si64(mm_res, dst2); // RED | GREEN -> mm_res - - // blue - src2 = src1; // src -> src2 - src2 = _mm_and_si64(src2, bmask); // src & MASKBLUE -> src2[000b 000b 000b 000b] - - dst2 = dst1; // dst -> dst2 - dst2 = _mm_and_si64(dst2, bmask); // dst & MASKBLUE -> dst2[000b 000b 000b 000b] - - // blend - src2 = _mm_sub_pi16(src2, dst2);// src - dst -> src2 - src2 = _mm_mullo_pi16(src2, mm_alpha); /* src2 * alpha -> src2 */ - src2 = _mm_srli_pi16(src2, 11); // src2 >> 11 -> src2 - dst2 = _mm_add_pi16(src2, dst2); // src2 + dst2 -> dst2 - dst2 = _mm_and_si64(dst2, bmask); // dst2 & MASKBLUE -> dst2 - - mm_res = _mm_or_si64(mm_res, dst2); // RED | GREEN | BLUE -> mm_res - - *(__m64*)dstp = mm_res; // mm_res -> 4 dst pixels - - srcp += 4; - dstp += 4; - }, width); - /* *INDENT-ON* */ // clang-format on - srcp += srcskip; - dstp += dstskip; - } - _mm_empty(); - } -} - -#endif // SDL_MMX_INTRINSICS - -// fast RGB565->RGB565 blending with surface alpha -static void Blit565to565SurfaceAlpha(SDL_BlitInfo *info) -{ - unsigned alpha = info->a; - if (alpha == 128) { - Blit16to16SurfaceAlpha128(info, 0xf7de); - } else { - int width = info->dst_w; - int height = info->dst_h; - Uint16 *srcp = (Uint16 *)info->src; - int srcskip = info->src_skip >> 1; - Uint16 *dstp = (Uint16 *)info->dst; - int dstskip = info->dst_skip >> 1; - alpha >>= 3; // downscale alpha to 5 bits - - while (height--) { - /* *INDENT-OFF* */ // clang-format off - DUFFS_LOOP({ - Uint32 s = *srcp++; - Uint32 d = *dstp; - /* - * shift out the middle component (green) to - * the high 16 bits, and process all three RGB - * components at the same time. - */ - s = (s | s << 16) & 0x07e0f81f; - d = (d | d << 16) & 0x07e0f81f; - d += (s - d) * alpha >> 5; - d &= 0x07e0f81f; - *dstp++ = (Uint16)(d | d >> 16); - }, width); - /* *INDENT-ON* */ // clang-format on - srcp += srcskip; - dstp += dstskip; - } - } -} - -// fast RGB555->RGB555 blending with surface alpha -static void Blit555to555SurfaceAlpha(SDL_BlitInfo *info) -{ - unsigned alpha = info->a; // downscale alpha to 5 bits - if (alpha == 128) { - Blit16to16SurfaceAlpha128(info, 0xfbde); - } else { - int width = info->dst_w; - int height = info->dst_h; - Uint16 *srcp = (Uint16 *)info->src; - int srcskip = info->src_skip >> 1; - Uint16 *dstp = (Uint16 *)info->dst; - int dstskip = info->dst_skip >> 1; - alpha >>= 3; // downscale alpha to 5 bits - - while (height--) { - /* *INDENT-OFF* */ // clang-format off - DUFFS_LOOP({ - Uint32 s = *srcp++; - Uint32 d = *dstp; - /* - * shift out the middle component (green) to - * the high 16 bits, and process all three RGB - * components at the same time. - */ - s = (s | s << 16) & 0x03e07c1f; - d = (d | d << 16) & 0x03e07c1f; - d += (s - d) * alpha >> 5; - d &= 0x03e07c1f; - *dstp++ = (Uint16)(d | d >> 16); - }, width); - /* *INDENT-ON* */ // clang-format on - srcp += srcskip; - dstp += dstskip; - } - } -} - -// fast ARGB8888->RGB565 blending with pixel alpha -static void BlitARGBto565PixelAlpha(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint32 *srcp = (Uint32 *)info->src; - int srcskip = info->src_skip >> 2; - Uint16 *dstp = (Uint16 *)info->dst; - int dstskip = info->dst_skip >> 1; - - while (height--) { - /* *INDENT-OFF* */ // clang-format off - DUFFS_LOOP({ - Uint32 s = *srcp; - unsigned alpha = s >> 27; // downscale alpha to 5 bits - /* Here we special-case opaque alpha since the - compositioning used (>>8 instead of /255) doesn't handle - it correctly. */ - if (alpha) { - if (alpha == (SDL_ALPHA_OPAQUE >> 3)) { - *dstp = (Uint16)((s >> 8 & 0xf800) + (s >> 5 & 0x7e0) + (s >> 3 & 0x1f)); - } else { - Uint32 d = *dstp; - /* - * convert source and destination to G0RAB65565 - * and blend all components at the same time - */ - s = ((s & 0xfc00) << 11) + (s >> 8 & 0xf800) + (s >> 3 & 0x1f); - d = (d | d << 16) & 0x07e0f81f; - d += (s - d) * alpha >> 5; - d &= 0x07e0f81f; - *dstp = (Uint16)(d | d >> 16); - } - } - srcp++; - dstp++; - }, width); - /* *INDENT-ON* */ // clang-format on - srcp += srcskip; - dstp += dstskip; - } -} - -// fast ARGB8888->RGB555 blending with pixel alpha -static void BlitARGBto555PixelAlpha(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint32 *srcp = (Uint32 *)info->src; - int srcskip = info->src_skip >> 2; - Uint16 *dstp = (Uint16 *)info->dst; - int dstskip = info->dst_skip >> 1; - - while (height--) { - /* *INDENT-OFF* */ // clang-format off - DUFFS_LOOP({ - unsigned alpha; - Uint32 s = *srcp; - alpha = s >> 27; // downscale alpha to 5 bits - /* Here we special-case opaque alpha since the - compositioning used (>>8 instead of /255) doesn't handle - it correctly. */ - if (alpha) { - if (alpha == (SDL_ALPHA_OPAQUE >> 3)) { - *dstp = (Uint16)((s >> 9 & 0x7c00) + (s >> 6 & 0x3e0) + (s >> 3 & 0x1f)); - } else { - Uint32 d = *dstp; - /* - * convert source and destination to G0RAB55555 - * and blend all components at the same time - */ - s = ((s & 0xf800) << 10) + (s >> 9 & 0x7c00) + (s >> 3 & 0x1f); - d = (d | d << 16) & 0x03e07c1f; - d += (s - d) * alpha >> 5; - d &= 0x03e07c1f; - *dstp = (Uint16)(d | d >> 16); - } - } - srcp++; - dstp++; - }, width); - /* *INDENT-ON* */ // clang-format on - srcp += srcskip; - dstp += dstskip; - } -} - -// General (slow) N->N blending with per-surface alpha -static void BlitNtoNSurfaceAlpha(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint8 *src = info->src; - int srcskip = info->src_skip; - Uint8 *dst = info->dst; - int dstskip = info->dst_skip; - const SDL_PixelFormatDetails *srcfmt = info->src_fmt; - const SDL_PixelFormatDetails *dstfmt = info->dst_fmt; - int srcbpp = srcfmt->bytes_per_pixel; - int dstbpp = dstfmt->bytes_per_pixel; - Uint32 Pixel; - unsigned sR, sG, sB; - unsigned dR, dG, dB, dA; - const unsigned sA = info->a; - - if (sA) { - while (height--) { - /* *INDENT-OFF* */ // clang-format off - DUFFS_LOOP( - { - DISEMBLE_RGB(src, srcbpp, srcfmt, Pixel, sR, sG, sB); - DISEMBLE_RGBA(dst, dstbpp, dstfmt, Pixel, dR, dG, dB, dA); - ALPHA_BLEND_RGBA(sR, sG, sB, sA, dR, dG, dB, dA); - ASSEMBLE_RGBA(dst, dstbpp, dstfmt, dR, dG, dB, dA); - src += srcbpp; - dst += dstbpp; - }, - width); - /* *INDENT-ON* */ // clang-format on - src += srcskip; - dst += dstskip; - } - } -} - -// General (slow) colorkeyed N->N blending with per-surface alpha -static void BlitNtoNSurfaceAlphaKey(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint8 *src = info->src; - int srcskip = info->src_skip; - Uint8 *dst = info->dst; - int dstskip = info->dst_skip; - const SDL_PixelFormatDetails *srcfmt = info->src_fmt; - const SDL_PixelFormatDetails *dstfmt = info->dst_fmt; - Uint32 ckey = info->colorkey; - int srcbpp = srcfmt->bytes_per_pixel; - int dstbpp = dstfmt->bytes_per_pixel; - Uint32 Pixel; - unsigned sR, sG, sB; - unsigned dR, dG, dB, dA; - const unsigned sA = info->a; - - while (height--) { - /* *INDENT-OFF* */ // clang-format off - DUFFS_LOOP( - { - RETRIEVE_RGB_PIXEL(src, srcbpp, Pixel); - if (sA && Pixel != ckey) { - RGB_FROM_PIXEL(Pixel, srcfmt, sR, sG, sB); - DISEMBLE_RGBA(dst, dstbpp, dstfmt, Pixel, dR, dG, dB, dA); - ALPHA_BLEND_RGBA(sR, sG, sB, sA, dR, dG, dB, dA); - ASSEMBLE_RGBA(dst, dstbpp, dstfmt, dR, dG, dB, dA); - } - src += srcbpp; - dst += dstbpp; - }, - width); - /* *INDENT-ON* */ // clang-format on - src += srcskip; - dst += dstskip; - } -} - -// Fast 32-bit RGBA->RGBA blending with pixel alpha -static void Blit8888to8888PixelAlpha(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint8 *src = info->src; - int srcskip = info->src_skip; - Uint8 *dst = info->dst; - int dstskip = info->dst_skip; - const SDL_PixelFormatDetails *srcfmt = info->src_fmt; - - while (height--) { - int i = 0; - - for (; i < width; ++i) { - Uint32 src32 = *(Uint32 *)src; - Uint32 dst32 = *(Uint32 *)dst; - ALPHA_BLEND_8888(src32, dst32, srcfmt); - *(Uint32 *)dst = dst32; - src += 4; - dst += 4; - } - - src += srcskip; - dst += dstskip; - } -} - -// Fast 32-bit RGBA->RGB(A) blending with pixel alpha and src swizzling -static void Blit8888to8888PixelAlphaSwizzle(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint8 *src = info->src; - int srcskip = info->src_skip; - Uint8 *dst = info->dst; - int dstskip = info->dst_skip; - const SDL_PixelFormatDetails *srcfmt = info->src_fmt; - const SDL_PixelFormatDetails *dstfmt = info->dst_fmt; - - while (height--) { - int i = 0; - - for (; i < width; ++i) { - Uint32 src32 = *(Uint32 *)src; - Uint32 dst32 = *(Uint32 *)dst; - ALPHA_BLEND_SWIZZLE_8888(src32, dst32, srcfmt, dstfmt); - *(Uint32 *)dst = dst32; - src += 4; - dst += 4; - } - - src += srcskip; - dst += dstskip; - } -} - -#ifdef SDL_SSE4_1_INTRINSICS - -static void SDL_TARGETING("sse4.1") Blit8888to8888PixelAlphaSwizzleSSE41(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint8 *src = info->src; - int srcskip = info->src_skip; - Uint8 *dst = info->dst; - int dstskip = info->dst_skip; - const SDL_PixelFormatDetails *srcfmt = info->src_fmt; - const SDL_PixelFormatDetails *dstfmt = info->dst_fmt; - - // The byte offsets for the start of each pixel - const __m128i mask_offsets = _mm_set_epi8( - 12, 12, 12, 12, 8, 8, 8, 8, 4, 4, 4, 4, 0, 0, 0, 0); - - const __m128i convert_mask = _mm_add_epi32( - _mm_set1_epi32( - ((srcfmt->Rshift >> 3) << dstfmt->Rshift) | - ((srcfmt->Gshift >> 3) << dstfmt->Gshift) | - ((srcfmt->Bshift >> 3) << dstfmt->Bshift)), - mask_offsets); - - const __m128i alpha_splat_mask = _mm_add_epi8(_mm_set1_epi8(srcfmt->Ashift >> 3), mask_offsets); - const __m128i alpha_fill_mask = _mm_set1_epi32((int)dstfmt->Amask); - - while (height--) { - int i = 0; - - for (; i + 4 <= width; i += 4) { - // Load 4 src pixels - __m128i src128 = _mm_loadu_si128((__m128i *)src); - - // Load 4 dst pixels - __m128i dst128 = _mm_loadu_si128((__m128i *)dst); - - // Extract the alpha from each pixel and splat it into all the channels - __m128i srcA = _mm_shuffle_epi8(src128, alpha_splat_mask); - - // Convert to dst format - src128 = _mm_shuffle_epi8(src128, convert_mask); - - // Set the alpha channels of src to 255 - src128 = _mm_or_si128(src128, alpha_fill_mask); - - // Duplicate each 8-bit alpha value into both bytes of 16-bit lanes - __m128i srca_lo = _mm_unpacklo_epi8(srcA, srcA); - __m128i srca_hi = _mm_unpackhi_epi8(srcA, srcA); - - // Calculate 255-srcA in every second 8-bit lane (255-srcA = srcA^0xff) - srca_lo = _mm_xor_si128(srca_lo, _mm_set1_epi16(0xff00)); - srca_hi = _mm_xor_si128(srca_hi, _mm_set1_epi16(0xff00)); - - // maddubs expects second argument to be signed, so subtract 128 - src128 = _mm_sub_epi8(src128, _mm_set1_epi8((Uint8)128)); - dst128 = _mm_sub_epi8(dst128, _mm_set1_epi8((Uint8)128)); - - // dst = srcA*(src-128) + (255-srcA)*(dst-128) = srcA*src + (255-srcA)*dst - 128*255 - __m128i dst_lo = _mm_maddubs_epi16(srca_lo, _mm_unpacklo_epi8(src128, dst128)); - __m128i dst_hi = _mm_maddubs_epi16(srca_hi, _mm_unpackhi_epi8(src128, dst128)); - - // dst += 0x1U (use 0x80 to round instead of floor) + 128*255 (to fix maddubs result) - dst_lo = _mm_add_epi16(dst_lo, _mm_set1_epi16(1 + 128*255)); - dst_hi = _mm_add_epi16(dst_hi, _mm_set1_epi16(1 + 128*255)); - - // dst = (dst + (dst >> 8)) >> 8 = (dst * 257) >> 16 - dst_lo = _mm_mulhi_epu16(dst_lo, _mm_set1_epi16(257)); - dst_hi = _mm_mulhi_epu16(dst_hi, _mm_set1_epi16(257)); - - // Blend the pixels together and save the result - _mm_storeu_si128((__m128i *)dst, _mm_packus_epi16(dst_lo, dst_hi)); - - src += 16; - dst += 16; - } - - for (; i < width; ++i) { - Uint32 src32 = *(Uint32 *)src; - Uint32 dst32 = *(Uint32 *)dst; - ALPHA_BLEND_SWIZZLE_8888(src32, dst32, srcfmt, dstfmt); - *(Uint32 *)dst = dst32; - src += 4; - dst += 4; - } - - src += srcskip; - dst += dstskip; - } -} - -#endif - -#ifdef SDL_AVX2_INTRINSICS - -static void SDL_TARGETING("avx2") Blit8888to8888PixelAlphaSwizzleAVX2(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint8 *src = info->src; - int srcskip = info->src_skip; - Uint8 *dst = info->dst; - int dstskip = info->dst_skip; - const SDL_PixelFormatDetails *srcfmt = info->src_fmt; - const SDL_PixelFormatDetails *dstfmt = info->dst_fmt; - - // The byte offsets for the start of each pixel - const __m256i mask_offsets = _mm256_set_epi8( - 28, 28, 28, 28, 24, 24, 24, 24, 20, 20, 20, 20, 16, 16, 16, 16, 12, 12, 12, 12, 8, 8, 8, 8, 4, 4, 4, 4, 0, 0, 0, 0); - - const __m256i convert_mask = _mm256_add_epi32( - _mm256_set1_epi32( - ((srcfmt->Rshift >> 3) << dstfmt->Rshift) | - ((srcfmt->Gshift >> 3) << dstfmt->Gshift) | - ((srcfmt->Bshift >> 3) << dstfmt->Bshift)), - mask_offsets); - - const __m256i alpha_splat_mask = _mm256_add_epi8(_mm256_set1_epi8(srcfmt->Ashift >> 3), mask_offsets); - const __m256i alpha_fill_mask = _mm256_set1_epi32((int)dstfmt->Amask); - - while (height--) { - int i = 0; - - for (; i + 8 <= width; i += 8) { - // Load 8 src pixels - __m256i src256 = _mm256_loadu_si256((__m256i *)src); - - // Load 8 dst pixels - __m256i dst256 = _mm256_loadu_si256((__m256i *)dst); - - // Extract the alpha from each pixel and splat it into all the channels - __m256i srcA = _mm256_shuffle_epi8(src256, alpha_splat_mask); - - // Convert to dst format - src256 = _mm256_shuffle_epi8(src256, convert_mask); - - // Set the alpha channels of src to 255 - src256 = _mm256_or_si256(src256, alpha_fill_mask); - - // Duplicate each 8-bit alpha value into both bytes of 16-bit lanes - __m256i alpha_lo = _mm256_unpacklo_epi8(srcA, srcA); - __m256i alpha_hi = _mm256_unpackhi_epi8(srcA, srcA); - - // Calculate 255-srcA in every second 8-bit lane (255-srcA = srcA^0xff) - alpha_lo = _mm256_xor_si256(alpha_lo, _mm256_set1_epi16(0xff00)); - alpha_hi = _mm256_xor_si256(alpha_hi, _mm256_set1_epi16(0xff00)); - - // maddubs expects second argument to be signed, so subtract 128 - src256 = _mm256_sub_epi8(src256, _mm256_set1_epi8((Uint8)128)); - dst256 = _mm256_sub_epi8(dst256, _mm256_set1_epi8((Uint8)128)); - - // dst = srcA*(src-128) + (255-srcA)*(dst-128) = srcA*src + (255-srcA)*dst - 128*255 - __m256i dst_lo = _mm256_maddubs_epi16(alpha_lo, _mm256_unpacklo_epi8(src256, dst256)); - __m256i dst_hi = _mm256_maddubs_epi16(alpha_hi, _mm256_unpackhi_epi8(src256, dst256)); - - // dst += 0x1U (use 0x80 to round instead of floor) + 128*255 (to fix maddubs result) - dst_lo = _mm256_add_epi16(dst_lo, _mm256_set1_epi16(1 + 128*255)); - dst_hi = _mm256_add_epi16(dst_hi, _mm256_set1_epi16(1 + 128*255)); - - // dst = (dst + (dst >> 8)) >> 8 = (dst * 257) >> 16 - dst_lo = _mm256_mulhi_epu16(dst_lo, _mm256_set1_epi16(257)); - dst_hi = _mm256_mulhi_epu16(dst_hi, _mm256_set1_epi16(257)); - - // Blend the pixels together and save the result - _mm256_storeu_si256((__m256i *)dst, _mm256_packus_epi16(dst_lo, dst_hi)); - - src += 32; - dst += 32; - } - - for (; i < width; ++i) { - Uint32 src32 = *(Uint32 *)src; - Uint32 dst32 = *(Uint32 *)dst; - ALPHA_BLEND_SWIZZLE_8888(src32, dst32, srcfmt, dstfmt); - *(Uint32 *)dst = dst32; - src += 4; - dst += 4; - } - - src += srcskip; - dst += dstskip; - } -} - -#endif - -#if defined(SDL_NEON_INTRINSICS) && (__ARM_ARCH >= 8) - -static void Blit8888to8888PixelAlphaSwizzleNEON(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint8 *src = info->src; - int srcskip = info->src_skip; - Uint8 *dst = info->dst; - int dstskip = info->dst_skip; - const SDL_PixelFormatDetails *srcfmt = info->src_fmt; - const SDL_PixelFormatDetails *dstfmt = info->dst_fmt; - - // The byte offsets for the start of each pixel - const uint8x16_t mask_offsets = vreinterpretq_u8_u64(vcombine_u64( - vcreate_u64(0x0404040400000000), vcreate_u64(0x0c0c0c0c08080808))); - - const uint8x16_t convert_mask = vreinterpretq_u8_u32(vaddq_u32( - vreinterpretq_u32_u8(mask_offsets), - vdupq_n_u32( - ((srcfmt->Rshift >> 3) << dstfmt->Rshift) | - ((srcfmt->Gshift >> 3) << dstfmt->Gshift) | - ((srcfmt->Bshift >> 3) << dstfmt->Bshift)))); - - const uint8x16_t alpha_splat_mask = vaddq_u8(vdupq_n_u8(srcfmt->Ashift >> 3), mask_offsets); - const uint8x16_t alpha_fill_mask = vreinterpretq_u8_u32(vdupq_n_u32(dstfmt->Amask)); - - while (height--) { - int i = 0; - - for (; i + 4 <= width; i += 4) { - // Load 4 src pixels - uint8x16_t src128 = vld1q_u8(src); - - // Load 4 dst pixels - uint8x16_t dst128 = vld1q_u8(dst); - - // Extract the alpha from each pixel and splat it into all the channels - uint8x16_t srcA = vqtbl1q_u8(src128, alpha_splat_mask); - - // Convert to dst format - src128 = vqtbl1q_u8(src128, convert_mask); - - // Set the alpha channels of src to 255 - src128 = vorrq_u8(src128, alpha_fill_mask); - - // 255 - srcA = ~srcA - uint8x16_t srcInvA = vmvnq_u8(srcA); - - // Result initialized with 1, this is for truncated divide later - uint16x8_t res_lo = vdupq_n_u16(1); - uint16x8_t res_hi = vdupq_n_u16(1); - - // res = alpha * src + (255 - alpha) * dst - res_lo = vmlal_u8(res_lo, vget_low_u8(srcA), vget_low_u8(src128)); - res_lo = vmlal_u8(res_lo, vget_low_u8(srcInvA), vget_low_u8(dst128)); - res_hi = vmlal_high_u8(res_hi, srcA, src128); - res_hi = vmlal_high_u8(res_hi, srcInvA, dst128); - - // Now result has +1 already added for truncated division - // dst = (res + (res >> 8)) >> 8 - uint8x8_t temp; - temp = vaddhn_u16(res_lo, vshrq_n_u16(res_lo, 8)); - dst128 = vaddhn_high_u16(temp, res_hi, vshrq_n_u16(res_hi, 8)); - - // For rounded division remove the constant 1 and change first two vmlal_u8 to vmull_u8 - // Then replace two previous lines with following code: - // temp = vraddhn_u16(res_lo, vrshrq_n_u16(res_lo, 8)); - // dst128 = vraddhn_high_u16(temp, res_hi, vrshrq_n_u16(res_hi, 8)); - - // Save the result - vst1q_u8(dst, dst128); - - src += 16; - dst += 16; - } - - // Process 1 pixel per iteration, max 3 iterations, same calculations as above - for (; i < width; ++i) { - // Top 32-bits will be not used in src32 & dst32 - uint8x8_t src32 = vreinterpret_u8_u32(vld1_dup_u32((Uint32*)src)); - uint8x8_t dst32 = vreinterpret_u8_u32(vld1_dup_u32((Uint32*)dst)); - - uint8x8_t srcA = vtbl1_u8(src32, vget_low_u8(alpha_splat_mask)); - src32 = vtbl1_u8(src32, vget_low_u8(convert_mask)); - src32 = vorr_u8(src32, vget_low_u8(alpha_fill_mask)); - uint8x8_t srcInvA = vmvn_u8(srcA); - - uint16x8_t res = vdupq_n_u16(1); - res = vmlal_u8(res, srcA, src32); - res = vmlal_u8(res, srcInvA, dst32); - - dst32 = vaddhn_u16(res, vshrq_n_u16(res, 8)); - - // Save the result, only low 32-bits - vst1_lane_u32((Uint32*)dst, vreinterpret_u32_u8(dst32), 0); - - src += 4; - dst += 4; - } - - src += srcskip; - dst += dstskip; - } -} - -#endif - -// General (slow) N->N blending with pixel alpha -static void BlitNtoNPixelAlpha(SDL_BlitInfo *info) -{ - int width = info->dst_w; - int height = info->dst_h; - Uint8 *src = info->src; - int srcskip = info->src_skip; - Uint8 *dst = info->dst; - int dstskip = info->dst_skip; - const SDL_PixelFormatDetails *srcfmt = info->src_fmt; - const SDL_PixelFormatDetails *dstfmt = info->dst_fmt; - int srcbpp; - int dstbpp; - Uint32 Pixel; - unsigned sR, sG, sB, sA; - unsigned dR, dG, dB, dA; - - // Set up some basic variables - srcbpp = srcfmt->bytes_per_pixel; - dstbpp = dstfmt->bytes_per_pixel; - - while (height--) { - DUFFS_LOOP( - { - DISEMBLE_RGBA(src, srcbpp, srcfmt, Pixel, sR, sG, sB, sA); - if (sA) { - DISEMBLE_RGBA(dst, dstbpp, dstfmt, Pixel, dR, dG, dB, dA); - ALPHA_BLEND_RGBA(sR, sG, sB, sA, dR, dG, dB, dA); - ASSEMBLE_RGBA(dst, dstbpp, dstfmt, dR, dG, dB, dA); - } - src += srcbpp; - dst += dstbpp; - }, - width); - /* *INDENT-ON* */ // clang-format on - src += srcskip; - dst += dstskip; - } -} - -SDL_BlitFunc SDL_CalculateBlitA(SDL_Surface *surface) -{ - const SDL_PixelFormatDetails *sf = surface->fmt; - const SDL_PixelFormatDetails *df = surface->map.info.dst_fmt; - - switch (surface->map.info.flags & ~SDL_COPY_RLE_MASK) { - case SDL_COPY_BLEND: - // Per-pixel alpha blits - switch (df->bytes_per_pixel) { - case 1: - if (surface->map.info.dst_pal) { - return BlitNto1PixelAlpha; - } else { - // RGB332 has no palette ! - return BlitNtoNPixelAlpha; - } - - case 2: - if (sf->bytes_per_pixel == 4 && sf->Amask == 0xff000000 && sf->Gmask == 0xff00 && ((sf->Rmask == 0xff && df->Rmask == 0x1f) || (sf->Bmask == 0xff && df->Bmask == 0x1f))) { - if (df->Gmask == 0x7e0) { - return BlitARGBto565PixelAlpha; - } else if (df->Gmask == 0x3e0 && !df->Amask) { - return BlitARGBto555PixelAlpha; - } - } - return BlitNtoNPixelAlpha; - - case 4: - if (SDL_PIXELLAYOUT(sf->format) == SDL_PACKEDLAYOUT_8888 && sf->Amask && - SDL_PIXELLAYOUT(df->format) == SDL_PACKEDLAYOUT_8888) { -#ifdef SDL_AVX2_INTRINSICS - if (SDL_HasAVX2()) { - return Blit8888to8888PixelAlphaSwizzleAVX2; - } -#endif -#ifdef SDL_SSE4_1_INTRINSICS - if (SDL_HasSSE41()) { - return Blit8888to8888PixelAlphaSwizzleSSE41; - } -#endif -#if defined(SDL_NEON_INTRINSICS) && (__ARM_ARCH >= 8) - // To prevent "unused function" compiler warnings/errors - (void)Blit8888to8888PixelAlpha; - (void)Blit8888to8888PixelAlphaSwizzle; - return Blit8888to8888PixelAlphaSwizzleNEON; -#else - if (sf->format == df->format) { - return Blit8888to8888PixelAlpha; - } else { - return Blit8888to8888PixelAlphaSwizzle; - } -#endif - } - return BlitNtoNPixelAlpha; - - case 3: - default: - break; - } - return BlitNtoNPixelAlpha; - - case SDL_COPY_MODULATE_ALPHA | SDL_COPY_BLEND: - if (sf->Amask == 0) { - // Per-surface alpha blits - switch (df->bytes_per_pixel) { - case 1: - if (surface->map.info.dst_pal) { - return BlitNto1SurfaceAlpha; - } else { - // RGB332 has no palette ! - return BlitNtoNSurfaceAlpha; - } - - case 2: - if (surface->map.identity) { - if (df->Gmask == 0x7e0) { -#ifdef SDL_MMX_INTRINSICS - if (SDL_HasMMX()) { - return Blit565to565SurfaceAlphaMMX; - } else -#endif - { - return Blit565to565SurfaceAlpha; - } - } else if (df->Gmask == 0x3e0) { -#ifdef SDL_MMX_INTRINSICS - if (SDL_HasMMX()) { - return Blit555to555SurfaceAlphaMMX; - } else -#endif - { - return Blit555to555SurfaceAlpha; - } - } - } - return BlitNtoNSurfaceAlpha; - - case 4: - if (sf->Rmask == df->Rmask && sf->Gmask == df->Gmask && sf->Bmask == df->Bmask && sf->bytes_per_pixel == 4) { -#ifdef SDL_SSE2_INTRINSICS - if (sf->Rshift % 8 == 0 && sf->Gshift % 8 == 0 && sf->Bshift % 8 == 0 && SDL_HasSSE2()) { - return Blit888to888SurfaceAlphaSSE2; - } -#endif - if ((sf->Rmask | sf->Gmask | sf->Bmask) == 0xffffff) { - return BlitRGBtoRGBSurfaceAlpha; - } - } - return BlitNtoNSurfaceAlpha; - - case 3: - default: - return BlitNtoNSurfaceAlpha; - } - } - break; - - case SDL_COPY_COLORKEY | SDL_COPY_MODULATE_ALPHA | SDL_COPY_BLEND: - if (sf->Amask == 0) { - if (df->bytes_per_pixel == 1) { - - if (surface->map.info.dst_pal) { - return BlitNto1SurfaceAlphaKey; - } else { - // RGB332 has no palette ! - return BlitNtoNSurfaceAlphaKey; - } - } else { - return BlitNtoNSurfaceAlphaKey; - } - } - break; - } - - return NULL; -} - -#endif // SDL_HAVE_BLIT_A - -- cgit v1.2.3