Mirrored_Repos/LookingGlass
1
0
Fork 0
mirror of https://github.com/gnif/LookingGlass.git synced 2026-08-02 05:12:02 +00:00
Code Issues Actions 2 Packages Projects Releases Wiki Activity

[common] rects: fix unaligned avx memcpy implementation

Browse Source
This commit is contained in:
Geoffrey McRae
2026-07-30 14:28:40 +10:00
parent f5dee45adc
commit 8828e640ab
1 changed files with 15 additions and 4 deletions
Download Patch File Download Diff File Expand all files Collapse all files

19
common/src/rects.c
View File

@@ -330,12 +330,20 @@ static void rectCopyUnaligned_avx(
src += ystart * srcPitch + dx; src += ystart * srcPitch + dx;
dst += ystart * dstPitch + dx; dst += ystart * dstPitch + dx;
const int align = (32 - ((uintptr_t)dst & 31)) & 31; bool streamed = false;
const int nvec = (width - align) / sizeof(__m256i);
const int rem = (width - align) % sizeof(__m256i);
for (int i = ystart; i < yend; ++i) for (int i = ystart; i < yend; ++i)
{ {
/*
* dstPitch is not necessarily a multiple of the AVX store alignment.
* Recalculate the prefix for every row so the streaming stores remain
* aligned for packed 24-bit and odd-width framebuffers.
*/
const int rowAlign = (32 - ((uintptr_t)dst & 31)) & 31;
const int align = min(rowAlign, width);
const int nvec = (width - align) / sizeof(__m256i);
const int rem = (width - align) % sizeof(__m256i);
streamed |= nvec > 0;
// copy the unaligned bytes // copy the unaligned bytes
for(int col = align - 1; col >= 0; --col) for(int col = align - 1; col >= 0; --col)
dst[col] = src[col]; dst[col] = src[col];
@@ -365,6 +373,9 @@ static void rectCopyUnaligned_avx(
src += srcPitch; src += srcPitch;
dst += dstPitch; dst += dstPitch;
} }
if (streamed)
_mm_sfence();
} }
#ifdef __clang__ #ifdef __clang__
#pragma clang attribute pop #pragma clang attribute pop