Emulator-Archive/ppsspp
1
0
Fork 0
mirror of https://github.com/hrydgard/ppsspp.git synced 2024-11-23 21:39:52 +00:00
Code Issues Actions 2 Packages Projects Releases Wiki Activity

softgpu: Use NEON for lighting.

Browse Source
This commit is contained in:
Unknown W. Brackets 2023-01-07 17:38:59 -08:00
parent 62fe03dcb4
commit 1215714240
1 changed files with 10 additions and 0 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

10
GPU/Software/Lighting.cpp
View File

@ -29,6 +29,10 @@ static inline Vec3f GetLightVec(const u32 lparams[12], int light) {
__m128i values = _mm_loadu_si128((__m128i *)&lparams[3 * light]); __m128i values = _mm_loadu_si128((__m128i *)&lparams[3 * light]);
__m128i from24 = _mm_slli_epi32(values, 8); __m128i from24 = _mm_slli_epi32(values, 8);
return _mm_castsi128_ps(from24); return _mm_castsi128_ps(from24);
#elif PPSSPP_ARCH(ARM64_NEON)
uint32x4_t values = vld1q_u32((uint32_t *)&lparams[3 * light]);
uint32x4_t from24 = vshlq_n_u32(values, 8);
return vreinterpretq_f32_u32(from24);
#else #else
return Vec3<float>(getFloat24(lparams[3 * light]), getFloat24(lparams[3 * light + 1]), getFloat24(lparams[3 * light + 2])); return Vec3<float>(getFloat24(lparams[3 * light]), getFloat24(lparams[3 * light + 1]), getFloat24(lparams[3 * light + 2]));
#endif #endif
@ -48,6 +52,8 @@ static inline float pspLightPow(float v, float e) {
static inline Vec4<int> LightColorFactor(const Vec4<int> &expanded, const Vec4<int> &ones) { static inline Vec4<int> LightColorFactor(const Vec4<int> &expanded, const Vec4<int> &ones) {
#if defined(_M_SSE) && !PPSSPP_ARCH(X86) #if defined(_M_SSE) && !PPSSPP_ARCH(X86)
return _mm_add_epi32(_mm_slli_epi32(expanded.ivec, 1), ones.ivec); return _mm_add_epi32(_mm_slli_epi32(expanded.ivec, 1), ones.ivec);
#elif PPSSPP_ARCH(ARM64_NEON)
return vaddq_s32(vshlq_n_s32(expanded.ivec, 1), ones.ivec);
#else #else
return expanded * 2 + ones; return expanded * 2 + ones;
#endif #endif
@ -62,6 +68,10 @@ static inline bool IsLargerThanHalf(const Vec4<int> &v) {
__m128i add23 = _mm_add_epi32(v.ivec, _mm_shuffle_epi32(v.ivec, _MM_SHUFFLE(3, 2, 3, 2))); __m128i add23 = _mm_add_epi32(v.ivec, _mm_shuffle_epi32(v.ivec, _MM_SHUFFLE(3, 2, 3, 2)));
__m128i add1 = _mm_add_epi32(add23, _mm_shuffle_epi32(add23, _MM_SHUFFLE(1, 1, 1, 1))); __m128i add1 = _mm_add_epi32(add23, _mm_shuffle_epi32(add23, _MM_SHUFFLE(1, 1, 1, 1)));
return _mm_cvtsi128_si32(add1) > 4; return _mm_cvtsi128_si32(add1) > 4;
#elif PPSSPP_ARCH(ARM64_NEON)
int32x2_t add02 = vpmax_s32(vget_low_s32(v.ivec), vget_high_s32(v.ivec));
int32x2_t add1 = vpmax_s32(add02, add02);
return vget_lane_s32(add1, 0) > 4;
#else #else
bool larger = false; bool larger = false;
for (int i = 0; i < 3; ++i) for (int i = 0; i < 3; ++i)