backup/cnc-ddraw
1
0
Fork 0
mirror of https://github.com/FunkyFr3sh/cnc-ddraw.git synced 2025-03-24 17:49:52 +01:00
Code Issues Projects Releases Activity

tweak avx copy

Browse Source
This commit is contained in:
FunkyFr3sh 2022-09-19 13:59:02 +02:00
parent f4ee6128c4
commit edec5da87c
1 changed files with 12 additions and 10 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

22
src/blt.c
View File

@ -14,27 +14,29 @@ void blt_copy(
#ifdef __AVX__ #ifdef __AVX__
if (size >= 1024 * 4096 && g_blt_use_avx && !((DWORD)dst % 32) && !((DWORD)src % 32)) if (size >= 1024 * 4096 && g_blt_use_avx && !((DWORD)dst % 32) && !((DWORD)src % 32))
{ {
_mm_prefetch((const char*)(src), _MM_HINT_NTA);
while (size >= 256) while (size >= 256)
{ {
__m256i c0 = _mm256_load_si256(((const __m256i*)src) + 0); __m256i c0 = _mm256_load_si256(((const __m256i*)src) + 0);
__m256i c1 = _mm256_load_si256(((const __m256i*)src) + 1); __m256i c1 = _mm256_load_si256(((const __m256i*)src) + 1);
__m256i c2 = _mm256_load_si256(((const __m256i*)src) + 2); __m256i c2 = _mm256_load_si256(((const __m256i*)src) + 2);
__m256i c3 = _mm256_load_si256(((const __m256i*)src) + 3); __m256i c3 = _mm256_load_si256(((const __m256i*)src) + 3);
__m256i c4 = _mm256_load_si256(((const __m256i*)src) + 4);
__m256i c5 = _mm256_load_si256(((const __m256i*)src) + 5);
__m256i c6 = _mm256_load_si256(((const __m256i*)src) + 6);
__m256i c7 = _mm256_load_si256(((const __m256i*)src) + 7);
_mm_prefetch((const char*)(src + 512), _MM_HINT_NTA);
_mm256_stream_si256((((__m256i*)dst) + 0), c0); _mm256_stream_si256((((__m256i*)dst) + 0), c0);
_mm256_stream_si256((((__m256i*)dst) + 1), c1); _mm256_stream_si256((((__m256i*)dst) + 1), c1);
_mm256_stream_si256((((__m256i*)dst) + 2), c2); _mm256_stream_si256((((__m256i*)dst) + 2), c2);
_mm256_stream_si256((((__m256i*)dst) + 3), c3); _mm256_stream_si256((((__m256i*)dst) + 3), c3);
_mm256_stream_si256((((__m256i*)dst) + 4), c4);
c0 = _mm256_load_si256(((const __m256i*)src) + 4); _mm256_stream_si256((((__m256i*)dst) + 5), c5);
c1 = _mm256_load_si256(((const __m256i*)src) + 5); _mm256_stream_si256((((__m256i*)dst) + 6), c6);
c2 = _mm256_load_si256(((const __m256i*)src) + 6); _mm256_stream_si256((((__m256i*)dst) + 7), c7);
c3 = _mm256_load_si256(((const __m256i*)src) + 7);
_mm256_stream_si256((((__m256i*)dst) + 4), c0);
_mm256_stream_si256((((__m256i*)dst) + 5), c1);
_mm256_stream_si256((((__m256i*)dst) + 6), c2);
_mm256_stream_si256((((__m256i*)dst) + 7), c3);
src += 256; src += 256;
dst += 256; dst += 256;