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

add AVX test code

Browse Source
This commit is contained in:
FunkyFr3sh 2022-09-18 19:02:15 +02:00
parent a1b58749a2
commit e8acc35f0d
2 changed files with 58 additions and 0 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

5
inc/blt.h
View File

@ -5,6 +5,11 @@
#include <windows.h>
void blt_copy(
unsigned char* dst,
unsigned char* src,
size_t size);
void blt_clean(
unsigned char* dst,
int dst_x,

53
src/blt.c
View File

@ -4,6 +4,59 @@
#include "blt.h"
void blt_copy(
unsigned char* dst,
unsigned char* src,
size_t size)
{
#ifdef __AVX__
if (size >= 1024 * 1536 && !((DWORD)dst % 32) && !((DWORD)src % 32))
{
while (size >= 256)
{
__m256i c0 = _mm256_load_si256(((const __m256i*)src) + 0);
__m256i c1 = _mm256_load_si256(((const __m256i*)src) + 1);
__m256i c2 = _mm256_load_si256(((const __m256i*)src) + 2);
__m256i c3 = _mm256_load_si256(((const __m256i*)src) + 3);
_mm256_stream_si256((((__m256i*)dst) + 0), c0);
_mm256_stream_si256((((__m256i*)dst) + 1), c1);
_mm256_stream_si256((((__m256i*)dst) + 2), c2);
_mm256_stream_si256((((__m256i*)dst) + 3), c3);
c0 = _mm256_load_si256(((const __m256i*)src) + 4);
c1 = _mm256_load_si256(((const __m256i*)src) + 5);
c2 = _mm256_load_si256(((const __m256i*)src) + 6);
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;
dst += 256;
size -= 256;
}
if (size > 0)
{
memcpy(dst, src, size);
}
return;
}
#endif
if (size >= 1024 * 100)
{
__movsb(dst, src, size);
}
else
{
memcpy(dst, src, size);
}
}
void blt_clean(
unsigned char* dst,
int dst_x,