commit 23848db74644f98e28b8bd1dda391123deeb43f2
author Marat Dukhan <maratek@google.com> Wed Aug 05 09:10:16 2020 -0700
committer XNNPACK Team <xnnpack-github-robot@google.com> Wed Aug 05 09:11:08 2020 -0700
tree d3415228a021d6f8d584383aeca461e16e70aac1
parent 2cc26222461a835b1e8d7451e7e4b0bd381dfd42

Reoptimize x86 requantization

PiperOrigin-RevId: 325031583

src/qs8-gemm/gen/2x8c8-xw-minmax-avx2.c

diff --git a/src/qs8-gemm/gen/2x8c8-xw-minmax-avx2.c b/src/qs8-gemm/gen/2x8c8-xw-minmax-avx2.c
index 3988477..2bcfc35 100644
--- a/src/qs8-gemm/gen/2x8c8-xw-minmax-avx2.c
+++ b/src/qs8-gemm/gen/2x8c8-xw-minmax-avx2.c
@@ -101,21 +101,21 @@
     const __m256i vacc0x02461357 = _mm256_hadd_epi32(vacc0x0213, vacc0x4657);
     const __m256i vacc1x02461357 = _mm256_hadd_epi32(vacc1x0213, vacc1x4657);
 
-    const __m256i vpermuate_mask = _mm256_set_epi32(7, 3, 6, 2, 5, 1, 4, 0);
-    __m256i vacc0x01234567 = _mm256_permutevar8x32_epi32(vacc0x02461357, vpermuate_mask);
-    __m256i vacc1x01234567 = _mm256_permutevar8x32_epi32(vacc1x02461357, vpermuate_mask);
+    const __m256i vpermute_mask = _mm256_set_epi32(7, 3, 6, 2, 5, 1, 4, 0);
+    __m256i vacc0x01234567 = _mm256_permutevar8x32_epi32(vacc0x02461357, vpermute_mask);
+    __m256i vacc1x01234567 = _mm256_permutevar8x32_epi32(vacc1x02461357, vpermute_mask);
 
     const __m256i vmultiplier = _mm256_broadcastsi128_si256(_mm_load_si128((const __m128i*) params->sse2.multiplier));
     const __m256i vrounding = _mm256_broadcastsi128_si256(_mm_load_si128((const __m128i*) params->sse2.rounding));
 
-    const __m256i vacc0x23016745 = _mm256_shuffle_epi32(vacc0x01234567, _MM_SHUFFLE(2, 3, 0, 1));
-    const __m256i vacc1x23016745 = _mm256_shuffle_epi32(vacc1x01234567, _MM_SHUFFLE(2, 3, 0, 1));
+    const __m256i vacc0x11335577 = _mm256_shuffle_epi32(vacc0x01234567, _MM_SHUFFLE(3, 3, 1, 1));
+    const __m256i vacc1x11335577 = _mm256_shuffle_epi32(vacc1x01234567, _MM_SHUFFLE(3, 3, 1, 1));
 
     const __m256i vprod0x0246 = _mm256_add_epi64(_mm256_mul_epi32(vacc0x01234567, vmultiplier), vrounding);
     const __m256i vprod1x0246 = _mm256_add_epi64(_mm256_mul_epi32(vacc1x01234567, vmultiplier), vrounding);
 
-    const __m256i vprod0x1357 = _mm256_add_epi64(_mm256_mul_epi32(vacc0x23016745, vmultiplier), vrounding);
-    const __m256i vprod1x1357 = _mm256_add_epi64(_mm256_mul_epi32(vacc1x23016745, vmultiplier), vrounding);
+    const __m256i vprod0x1357 = _mm256_add_epi64(_mm256_mul_epi32(vacc0x11335577, vmultiplier), vrounding);
+    const __m256i vprod1x1357 = _mm256_add_epi64(_mm256_mul_epi32(vacc1x11335577, vmultiplier), vrounding);
 
     const __m256i vq31prod0x0246 = _mm256_srli_epi64(vprod0x0246, 31);
     const __m256i vq31prod0x1357 = _mm256_add_epi64(vprod0x1357, vprod0x1357);