mirror/RetroArch
1
0
Fork 0
mirror of https://github.com/libretro/RetroArch synced 2025-04-10 06:44:27 +00:00
Code Issues Packages Projects Releases Wiki Activity

(libretro-common) Resync

Browse Source
This commit is contained in:
libretroadmin 2023-05-30 19:34:55 +02:00
parent 119230e84b
commit 72bd1a2ba4
1 changed files with 40 additions and 0 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

40
libretro-common/gfx/scaler/pixconv.c
View File

@ -41,6 +41,8 @@
#include <emmintrin.h> #include <emmintrin.h>
#elif defined(__MMX__) #elif defined(__MMX__)
#include <mmintrin.h> #include <mmintrin.h>
#elif (defined(__ARM_NEON__) || defined(__ARM_NEON))
#include <arm_neon.h>
#endif #endif
void conv_rgb565_0rgb1555(void *output_, const void *input_, void conv_rgb565_0rgb1555(void *output_, const void *input_,
@ -220,6 +222,8 @@ void conv_rgb565_argb8888(void *output_, const void *input_,
const __m64 a = _mm_set1_pi16(0x00ff); const __m64 a = _mm_set1_pi16(0x00ff);
int max_width = width - 3; int max_width = width - 3;
#elif (defined(__ARM_NEON__) || defined(__ARM_NEON))
int max_width = width - 7;
#endif #endif
for (h = 0; h < height; for (h = 0; h < height;
@ -282,6 +286,23 @@ void conv_rgb565_argb8888(void *output_, const void *input_,
} }
_mm_empty(); _mm_empty();
#elif (defined(__ARM_NEON__) || defined(__ARM_NEON))
for (; w < max_width; w += 8)
{
uint16x8_t in = vld1q_u16(input + w);
uint16x8_t r = vsriq_n_u16(in, in, 5);
uint16x8_t b = vsliq_n_u16(in, in, 5);
uint16x8_t g = vsriq_n_u16(b, b, 6);
uint8x8x4_t res;
res.val[3] = vdup_n_u8(0xffu);
res.val[2] = vshrn_n_u16(r, 8);
res.val[1] = vshrn_n_u16(g, 8);
res.val[0] = vshrn_n_u16(b, 2);
vst4_u8((uint8_t*)(output + w), res);
}
#endif #endif
for (; w < width; w++) for (; w < width; w++)
@ -315,6 +336,8 @@ void conv_rgb565_abgr8888(void *output_, const void *input_,
const __m128i mul16_b = _mm_set1_epi16(0x4200); const __m128i mul16_b = _mm_set1_epi16(0x4200);
const __m128i a = _mm_set1_epi16(0x00ff); const __m128i a = _mm_set1_epi16(0x00ff);
int max_width = width - 7; int max_width = width - 7;
#elif (defined(__ARM_NEON__) || defined(__ARM_NEON))
int max_width = width - 7;
#endif #endif
for (h = 0; h < height; for (h = 0; h < height;
h++, output += out_stride >> 2, input += in_stride >> 1) h++, output += out_stride >> 2, input += in_stride >> 1)
@ -343,6 +366,23 @@ void conv_rgb565_abgr8888(void *output_, const void *input_,
_mm_storeu_si128((__m128i*)(output + w + 0), res_lo); _mm_storeu_si128((__m128i*)(output + w + 0), res_lo);
_mm_storeu_si128((__m128i*)(output + w + 4), res_hi); _mm_storeu_si128((__m128i*)(output + w + 4), res_hi);
} }
#elif (defined(__ARM_NEON__) || defined(__ARM_NEON))
for (; w < max_width; w += 8)
{
uint16x8_t in = vld1q_u16(input + w);
uint16x8_t r = vsriq_n_u16(in, in, 5);
uint16x8_t b = vsliq_n_u16(in, in, 5);
uint16x8_t g = vsriq_n_u16(b, b, 6);
uint8x8x4_t res;
res.val[3] = vdup_n_u8(0xffu);
res.val[2] = vshrn_n_u16(b, 2);
res.val[1] = vshrn_n_u16(g, 8);
res.val[0] = vshrn_n_u16(r, 8);
vst4_u8((uint8_t*)(output + w), res);
}
#endif #endif
for (; w < width; w++) for (; w < width; w++)
{ {