ShuriZma
/
flycast
mirror of https://github.com/flyinghead/flycast.git
1
0
Fork 0
Code Issues Packages Projects Releases Wiki Activity

Cleanup/optimize ta_thd_data32_i 

- Use 128-byte copies
- read pcw from memory
This commit is contained in:
Stefanos Kornilios Mitsis Poiitidis 2017-04-25 13:20:33 +02:00
parent 90395f099e
commit 8e3b9b434c
1 changed files with 32 additions and 18 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

50
core/hw/pvr/ta.cpp
View File

@ -18,7 +18,19 @@ extern u32 SQW,DMAW;
#else
#define SQWC(x)
#define DMAWC(x)
#endif
#if HOST_CPU == CPU_X86
#include <xmmintrin.h>
typedef __m128 simd128_t;
#elif HOST_CPU == CPU_ARM && defined(__ARM_NEON__)
#include <arm_neon.h>
typedef uint64x2_t simd128_t;
#else
struct simd128_t
{
DECL_ALIGN(32) u64 data[2];
};
#endif
/*
@ -273,34 +285,36 @@ void ta_vtx_SoftReset()
ta_cur_state=TAS_NS;
}
INLINE
void DYNACALL ta_thd_data32_i(void* data)
{
f64* dst=(f64*)ta_tad.thd_data;
f64* src=(f64*)data;
{
simd128_t* dst = (simd128_t*)ta_tad.thd_data;
simd128_t* src = (simd128_t*)data;
ta_tad.thd_data+=32;
PCW pcw = *(PCW*)src;
dst[0] = src[0];
dst[1] = src[1];
f64 t = src[0];
dst[0]=t;
dst[1]=src[1];
dst[2]=src[2];
dst[3]=src[3];
ta_tad.thd_data += 32;
PCW pcw=(PCW&)t;
u32 state_in = (ta_cur_state<<8) | (pcw.ParaType<<5) | (pcw.obj_ctrl>>2)%32;
u8 trans = ta_fsm[state_in];
ta_cur_state = (ta_state)trans;
bool must_handle=trans&0xF0;
u32 state_in = (ta_cur_state << 8) | (pcw.ParaType << 5) | ((pcw.obj_ctrl >> 2) & 31);
u32 trans = ta_fsm[state_in];
ta_cur_state = (ta_state)trans;
bool must_handle = trans & 0xF0;
if (unlikely(must_handle))
if (!unlikely(must_handle))
{
return;
}
else
{
ta_handle_cmd(trans);
}
}
void DYNACALL ta_vtx_data32(void* data)
{
SQWC(1);