Use lddqu instead of loadu since it may perform better in certain sit…

…uations Signed-off-by: João Silva <jgc3silva@gmail.com>
jgaeddert · May 19, 2024 · ea58420 · ea58420
1 parent 7a07f99
commit ea58420
Show file tree

Hide file tree

Showing 2 changed files with 5 additions and 5 deletions.
diff --git a/src/random/src/scramble.avx.c b/src/random/src/scramble.avx.c
@@ -47,7 +47,7 @@ void scramble_data(unsigned char * _x,
     // apply static masks
     unsigned int i;
     for (i=0; i<t; i+=32) {
-        x = _mm256_loadu_si256((const __m256i_u *)&_x[i]);
+        x = _mm256_lddqu_si256((const __m256i_u *)&_x[i]);
 
 #if HAVE_AVX2
         x = _mm256_xor_si256(x, mask);
@@ -97,7 +97,7 @@ void unscramble_data_soft(unsigned char * _x,
     // apply static masks
     unsigned int i;
     for (i=0; i<t; i+=4) {
-        x = _mm256_loadu_si256((const __m256i_u *)&_x[8 * i]);
+        x = _mm256_lddqu_si256((const __m256i_u *)&_x[8 * i]);
         y = _mm256_sub_epi8(mask, x);
         x = _mm256_blendv_epi8(x, y, mask);
         _mm256_storeu_si256((__m256i_u *)&_x[8 * i], x);

diff --git a/src/random/src/scramble.sse.c b/src/random/src/scramble.sse.c
@@ -49,7 +49,7 @@ void scramble_data(unsigned char * _x,
     // apply static masks
     unsigned int i;
     for (i=0; i<t; i+=16) {
-        x = _mm_loadu_si128((const __m128i_u *)&_x[i]);
+        x = _mm_lddqu_si128((const __m128i_u *)&_x[i]);
 
         x = _mm_xor_si128(x, mask);
 
@@ -96,12 +96,12 @@ void unscramble_data_soft(unsigned char * _x,
     // apply static masks
     unsigned int i;
     for (i=0; i<t; i+=4) {
-        x = _mm_loadu_si128((const __m128i_u *)&_x[8 * i]);
+        x = _mm_lddqu_si128((const __m128i_u *)&_x[8 * i]);
         y = _mm_sub_epi8(mask01, x);
         x = _mm_blendv_epi8(x, y, mask01);
         _mm_storeu_si128((__m128i_u *)&_x[8 * i], x);
 
-        x = _mm_loadu_si128((const __m128i_u *)&_x[8 * i + 16]);
+        x = _mm_lddqu_si128((const __m128i_u *)&_x[8 * i + 16]);
         y = _mm_sub_epi8(mask23, x);
         x = _mm_blendv_epi8(x, y, mask23);
         _mm_storeu_si128((__m128i_u *)&_x[8 * i + 16], x);