jirayu_sri/stockfish
1
0
Fork 0
mirror of https://github.com/official-stockfish/Stockfish.git synced 2026-07-22 12:47:08 +00:00
Code Issues Packages Projects Releases Wiki Activity

AVX-512 squared clipped ReLU

Browse Source 
Passed STC:
https://tests.stockfishchess.org/tests/view/6a4dd1075529b8472df7fd5e
LLR: 3.44 (-2.94,2.94) <0.00,2.00>
Total: 327136 W: 84861 L: 84124 D: 158151
Ptnml(0-2): 692, 34323, 92827, 35008, 718

closes https://github.com/official-stockfish/Stockfish/pull/6974

No functional change
This commit is contained in:
Linmiao Xu
2026-07-16 08:28:24 +02:00
committed by Joost VandeVondele
parent 8ddea72917
commit 4c78ba8920
1 changed files with 18 additions and 1 deletions
Download Patch File Download Diff File Expand all files Collapse all files
src/nnue/layers/sqr_clipped_relu.h
+18 -1
View File
@@ -75,7 +75,24 @@ class SqrClippedReLU {
// MulHi strips the lower 16 bits (i.e. shift by 16) so we need to shift out the remaining. // MulHi strips the lower 16 bits (i.e. shift by 16) so we need to shift out the remaining.
[[maybe_unused]] constexpr int SimdShiftAmount = WeightScaleBitsLocal * 2 + 7 - 16; [[maybe_unused]] constexpr int SimdShiftAmount = WeightScaleBitsLocal * 2 + 7 - 16;
#if defined(USE_SSE2) #if defined(USE_AVX512)
static_assert(InputDimensions % 32 == 0);
constexpr IndexType NumChunks = InputDimensions / 32;
const auto in = reinterpret_cast<const __m512i*>(input);
const auto out = reinterpret_cast<__m256i*>(output);
for (IndexType i = 0; i < NumChunks; ++i)
{
const __m256i words0 = _mm512_cvtsepi32_epi16(_mm512_load_si512(&in[i * 2 + 0]));
const __m256i words1 = _mm512_cvtsepi32_epi16(_mm512_load_si512(&in[i * 2 + 1]));
__m512i words = _mm512_inserti64x4(_mm512_castsi256_si512(words0), words1, 1);
words = _mm512_srli_epi16(_mm512_mulhi_epi16(words, words), SimdShiftAmount);
_mm256_store_si256(&out[i], _mm512_cvtsepi16_epi8(words));
}
constexpr IndexType Start = NumChunks * 32;
#elif defined(USE_SSE2)
constexpr IndexType NumChunks = InputDimensions / 16; constexpr IndexType NumChunks = InputDimensions / 16;
const auto in = reinterpret_cast<const __m128i*>(input); const auto in = reinterpret_cast<const __m128i*>(input);
const auto out = reinterpret_cast<__m128i*>(output); const auto out = reinterpret_cast<__m128i*>(output);