Compiler Explorer

Source code

#include <assert.h>
#include <immintrin.h>
#include <stdint.h>
#include <sys/random.h>

#include <immintrin.h>
#include <stdint.h>

template <uint8_t Imm>
static __m128i tern(__m128i a, __m128i b, __m128i c, __m128i d) {
  return _mm_ternarylogic_epi32(a, b, c, Imm);
}

template <uint8_t Imm>
static __m128i tern_asm(__m128i a, __m128i b, __m128i c, __m128i d) {
  __asm__ volatile("vpternlogd %[Imm], %[c], %[b], %[a]\n"
                   : [a] "+v"(a)
                   : [b] "v"(b), [c] "v"(c), [Imm] "i"(Imm)
                   :);
  return a;
}

__attribute__((noinline)) __m128i ternN(__m128i a, __m128i b, __m128i c,
                                        __m128i d, uint8_t Imm) {
  switch (Imm) {
  case 0x0:
    return tern<0x0>(a, b, c, d);
  case 0x1:
    return tern<0x1>(a, b, c, d);
  case 0x2:
    return tern<0x2>(a, b, c, d);
  case 0x3:
    return tern<0x3>(a, b, c, d);
  case 0x4:
    return tern<0x4>(a, b, c, d);
  case 0x5:
    return tern<0x5>(a, b, c, d);
  case 0x6:
    return tern<0x6>(a, b, c, d);
  case 0x7:
    return tern<0x7>(a, b, c, d);
  case 0x8:
    return tern<0x8>(a, b, c, d);
  case 0x9:
    return tern<0x9>(a, b, c, d);
  case 0xa:
    return tern<0xa>(a, b, c, d);
  case 0xb:
    return tern<0xb>(a, b, c, d);
  case 0xc:
    return tern<0xc>(a, b, c, d);
  case 0xd:
    return tern<0xd>(a, b, c, d);
  case 0xe:
    return tern<0xe>(a, b, c, d);
  case 0xf:
    return tern<0xf>(a, b, c, d);
  case 0x10:
    return tern<0x10>(a, b, c, d);
  case 0x11:
    return tern<0x11>(a, b, c, d);
  case 0x12:
    return tern<0x12>(a, b, c, d);
  case 0x13:
    return tern<0x13>(a, b, c, d);
  case 0x14:
    return tern<0x14>(a, b, c, d);
  case 0x15:
    return tern<0x15>(a, b, c, d);
  case 0x16:
    return tern<0x16>(a, b, c, d);
  case 0x17:
    return tern<0x17>(a, b, c, d);
  case 0x18:
    return tern<0x18>(a, b, c, d);
  case 0x19:
    return tern<0x19>(a, b, c, d);
  case 0x1a:
    return tern<0x1a>(a, b, c, d);
  case 0x1b:
    return tern<0x1b>(a, b, c, d);
  case 0x1c:
    return tern<0x1c>(a, b, c, d);
  case 0x1d:
    return tern<0x1d>(a, b, c, d);
  case 0x1e:
    return tern<0x1e>(a, b, c, d);
  case 0x1f:
    return tern<0x1f>(a, b, c, d);
  case 0x20:
    return tern<0x20>(a, b, c, d);
  case 0x21:
    return tern<0x21>(a, b, c, d);
  case 0x22:
    return tern<0x22>(a, b, c, d);
  case 0x23:
    return tern<0x23>(a, b, c, d);
  case 0x24:
    return tern<0x24>(a, b, c, d);
  case 0x25:
    return tern<0x25>(a, b, c, d);
  case 0x26:
    return tern<0x26>(a, b, c, d);
  case 0x27:
    return tern<0x27>(a, b, c, d);
  case 0x28:
    return tern<0x28>(a, b, c, d);
  case 0x29:
    return tern<0x29>(a, b, c, d);
  case 0x2a:
    return tern<0x2a>(a, b, c, d);
  case 0x2b:
    return tern<0x2b>(a, b, c, d);
  case 0x2c:
    return tern<0x2c>(a, b, c, d);
  case 0x2d:
    return tern<0x2d>(a, b, c, d);
  case 0x2e:
    return tern<0x2e>(a, b, c, d);
  case 0x2f:
    return tern<0x2f>(a, b, c, d);
  case 0x30:
    return tern<0x30>(a, b, c, d);
  case 0x31:
    return tern<0x31>(a, b, c, d);
  case 0x32:
    return tern<0x32>(a, b, c, d);
  case 0x33:
    return tern<0x33>(a, b, c, d);
  case 0x34:
    return tern<0x34>(a, b, c, d);
  case 0x35:
    return tern<0x35>(a, b, c, d);
  case 0x36:
    return tern<0x36>(a, b, c, d);
  case 0x37:
    return tern<0x37>(a, b, c, d);
  case 0x38:
    return tern<0x38>(a, b, c, d);
  case 0x39:
    return tern<0x39>(a, b, c, d);
  case 0x3a:
    return tern<0x3a>(a, b, c, d);
  case 0x3b:
    return tern<0x3b>(a, b, c, d);
  case 0x3c:
    return tern<0x3c>(a, b, c, d);
  case 0x3d:
    return tern<0x3d>(a, b, c, d);
  case 0x3e:
    return tern<0x3e>(a, b, c, d);
  case 0x3f:
    return tern<0x3f>(a, b, c, d);
  case 0x40:
    return tern<0x40>(a, b, c, d);
  case 0x41:
    return tern<0x41>(a, b, c, d);
  case 0x42:
    return tern<0x42>(a, b, c, d);
  case 0x43:
    return tern<0x43>(a, b, c, d);
  case 0x44:
    return tern<0x44>(a, b, c, d);
  case 0x45:
    return tern<0x45>(a, b, c, d);
  case 0x46:
    return tern<0x46>(a, b, c, d);
  case 0x47:
    return tern<0x47>(a, b, c, d);
  case 0x48:
    return tern<0x48>(a, b, c, d);
  case 0x49:
    return tern<0x49>(a, b, c, d);
  case 0x4a:
    return tern<0x4a>(a, b, c, d);
  case 0x4b:
    return tern<0x4b>(a, b, c, d);
  case 0x4c:
    return tern<0x4c>(a, b, c, d);
  case 0x4d:
    return tern<0x4d>(a, b, c, d);
  case 0x4e:
    return tern<0x4e>(a, b, c, d);
  case 0x4f:
    return tern<0x4f>(a, b, c, d);
  case 0x50:
    return tern<0x50>(a, b, c, d);
  case 0x51:
    return tern<0x51>(a, b, c, d);
  case 0x52:
    return tern<0x52>(a, b, c, d);
  case 0x53:
    return tern<0x53>(a, b, c, d);
  case 0x54:
    return tern<0x54>(a, b, c, d);
  case 0x55:
    return tern<0x55>(a, b, c, d);
  case 0x56:
    return tern<0x56>(a, b, c, d);
  case 0x57:
    return tern<0x57>(a, b, c, d);
  case 0x58:
    return tern<0x58>(a, b, c, d);
  case 0x59:
    return tern<0x59>(a, b, c, d);
  case 0x5a:
    return tern<0x5a>(a, b, c, d);
  case 0x5b:
    return tern<0x5b>(a, b, c, d);
  case 0x5c:
    return tern<0x5c>(a, b, c, d);
  case 0x5d:
    return tern<0x5d>(a, b, c, d);
  case 0x5e:
    return tern<0x5e>(a, b, c, d);
  case 0x5f:
    return tern<0x5f>(a, b, c, d);
  case 0x60:
    return tern<0x60>(a, b, c, d);
  case 0x61:
    return tern<0x61>(a, b, c, d);
  case 0x62:
    return tern<0x62>(a, b, c, d);
  case 0x63:
    return tern<0x63>(a, b, c, d);
  case 0x64:
    return tern<0x64>(a, b, c, d);
  case 0x65:
    return tern<0x65>(a, b, c, d);
  case 0x66:
    return tern<0x66>(a, b, c, d);
  case 0x67:
    return tern<0x67>(a, b, c, d);
  case 0x68:
    return tern<0x68>(a, b, c, d);
  case 0x69:
    return tern<0x69>(a, b, c, d);
  case 0x6a:
    return tern<0x6a>(a, b, c, d);
  case 0x6b:
    return tern<0x6b>(a, b, c, d);
  case 0x6c:
    return tern<0x6c>(a, b, c, d);
  case 0x6d:
    return tern<0x6d>(a, b, c, d);
  case 0x6e:
    return tern<0x6e>(a, b, c, d);
  case 0x6f:
    return tern<0x6f>(a, b, c, d);
  case 0x70:
    return tern<0x70>(a, b, c, d);
  case 0x71:
    return tern<0x71>(a, b, c, d);
  case 0x72:
    return tern<0x72>(a, b, c, d);
  case 0x73:
    return tern<0x73>(a, b, c, d);
  case 0x74:
    return tern<0x74>(a, b, c, d);
  case 0x75:
    return tern<0x75>(a, b, c, d);
  case 0x76:
    return tern<0x76>(a, b, c, d);
  case 0x77:
    return tern<0x77>(a, b, c, d);
  case 0x78:
    return tern<0x78>(a, b, c, d);
  case 0x79:
    return tern<0x79>(a, b, c, d);
  case 0x7a:
    return tern<0x7a>(a, b, c, d);
  case 0x7b:
    return tern<0x7b>(a, b, c, d);
  case 0x7c:
    return tern<0x7c>(a, b, c, d);
  case 0x7d:
    return tern<0x7d>(a, b, c, d);
  case 0x7e:
    return tern<0x7e>(a, b, c, d);
  case 0x7f:
    return tern<0x7f>(a, b, c, d);
  case 0x80:
    return tern<0x80>(a, b, c, d);
  case 0x81:
    return tern<0x81>(a, b, c, d);
  case 0x82:
    return tern<0x82>(a, b, c, d);
  case 0x83:
    return tern<0x83>(a, b, c, d);
  case 0x84:
    return tern<0x84>(a, b, c, d);
  case 0x85:
    return tern<0x85>(a, b, c, d);
  case 0x86:
    return tern<0x86>(a, b, c, d);
  case 0x87:
    return tern<0x87>(a, b, c, d);
  case 0x88:
    return tern<0x88>(a, b, c, d);
  case 0x89:
    return tern<0x89>(a, b, c, d);
  case 0x8a:
    return tern<0x8a>(a, b, c, d);
  case 0x8b:
    return tern<0x8b>(a, b, c, d);
  case 0x8c:
    return tern<0x8c>(a, b, c, d);
  case 0x8d:
    return tern<0x8d>(a, b, c, d);
  case 0x8e:
    return tern<0x8e>(a, b, c, d);
  case 0x8f:
    return tern<0x8f>(a, b, c, d);
  case 0x90:
    return tern<0x90>(a, b, c, d);
  case 0x91:
    return tern<0x91>(a, b, c, d);
  case 0x92:
    return tern<0x92>(a, b, c, d);
  case 0x93:
    return tern<0x93>(a, b, c, d);
  case 0x94:
    return tern<0x94>(a, b, c, d);
  case 0x95:
    return tern<0x95>(a, b, c, d);
  case 0x96:
    return tern<0x96>(a, b, c, d);
  case 0x97:
    return tern<0x97>(a, b, c, d);
  case 0x98:
    return tern<0x98>(a, b, c, d);
  case 0x99:
    return tern<0x99>(a, b, c, d);
  case 0x9a:
    return tern<0x9a>(a, b, c, d);
  case 0x9b:
    return tern<0x9b>(a, b, c, d);
  case 0x9c:
    return tern<0x9c>(a, b, c, d);
  case 0x9d:
    return tern<0x9d>(a, b, c, d);
  case 0x9e:
    return tern<0x9e>(a, b, c, d);
  case 0x9f:
    return tern<0x9f>(a, b, c, d);
  case 0xa0:
    return tern<0xa0>(a, b, c, d);
  case 0xa1:
    return tern<0xa1>(a, b, c, d);
  case 0xa2:
    return tern<0xa2>(a, b, c, d);
  case 0xa3:
    return tern<0xa3>(a, b, c, d);
  case 0xa4:
    return tern<0xa4>(a, b, c, d);
  case 0xa5:
    return tern<0xa5>(a, b, c, d);
  case 0xa6:
    return tern<0xa6>(a, b, c, d);
  case 0xa7:
    return tern<0xa7>(a, b, c, d);
  case 0xa8:
    return tern<0xa8>(a, b, c, d);
  case 0xa9:
    return tern<0xa9>(a, b, c, d);
  case 0xaa:
    return tern<0xaa>(a, b, c, d);
  case 0xab:
    return tern<0xab>(a, b, c, d);
  case 0xac:
    return tern<0xac>(a, b, c, d);
  case 0xad:
    return tern<0xad>(a, b, c, d);
  case 0xae:
    return tern<0xae>(a, b, c, d);
  case 0xaf:
    return tern<0xaf>(a, b, c, d);
  case 0xb0:
    return tern<0xb0>(a, b, c, d);
  case 0xb1:
    return tern<0xb1>(a, b, c, d);
  case 0xb2:
    return tern<0xb2>(a, b, c, d);
  case 0xb3:
    return tern<0xb3>(a, b, c, d);
  case 0xb4:
    return tern<0xb4>(a, b, c, d);
  case 0xb5:
    return tern<0xb5>(a, b, c, d);
  case 0xb6:
    return tern<0xb6>(a, b, c, d);
  case 0xb7:
    return tern<0xb7>(a, b, c, d);
  case 0xb8:
    return tern<0xb8>(a, b, c, d);
  case 0xb9:
    return tern<0xb9>(a, b, c, d);
  case 0xba:
    return tern<0xba>(a, b, c, d);
  case 0xbb:
    return tern<0xbb>(a, b, c, d);
  case 0xbc:
    return tern<0xbc>(a, b, c, d);
  case 0xbd:
    return tern<0xbd>(a, b, c, d);
  case 0xbe:
    return tern<0xbe>(a, b, c, d);
  case 0xbf:
    return tern<0xbf>(a, b, c, d);
  case 0xc0:
    return tern<0xc0>(a, b, c, d);
  case 0xc1:
    return tern<0xc1>(a, b, c, d);
  case 0xc2:
    return tern<0xc2>(a, b, c, d);
  case 0xc3:
    return tern<0xc3>(a, b, c, d);
  case 0xc4:
    return tern<0xc4>(a, b, c, d);
  case 0xc5:
    return tern<0xc5>(a, b, c, d);
  case 0xc6:
    return tern<0xc6>(a, b, c, d);
  case 0xc7:
    return tern<0xc7>(a, b, c, d);
  case 0xc8:
    return tern<0xc8>(a, b, c, d);
  case 0xc9:
    return tern<0xc9>(a, b, c, d);
  case 0xca:
    return tern<0xca>(a, b, c, d);
  case 0xcb:
    return tern<0xcb>(a, b, c, d);
  case 0xcc:
    return tern<0xcc>(a, b, c, d);
  case 0xcd:
    return tern<0xcd>(a, b, c, d);
  case 0xce:
    return tern<0xce>(a, b, c, d);
  case 0xcf:
    return tern<0xcf>(a, b, c, d);
  case 0xd0:
    return tern<0xd0>(a, b, c, d);
  case 0xd1:
    return tern<0xd1>(a, b, c, d);
  case 0xd2:
    return tern<0xd2>(a, b, c, d);
  case 0xd3:
    return tern<0xd3>(a, b, c, d);
  case 0xd4:
    return tern<0xd4>(a, b, c, d);
  case 0xd5:
    return tern<0xd5>(a, b, c, d);
  case 0xd6:
    return tern<0xd6>(a, b, c, d);
  case 0xd7:
    return tern<0xd7>(a, b, c, d);
  case 0xd8:
    return tern<0xd8>(a, b, c, d);
  case 0xd9:
    return tern<0xd9>(a, b, c, d);
  case 0xda:
    return tern<0xda>(a, b, c, d);
  case 0xdb:
    return tern<0xdb>(a, b, c, d);
  case 0xdc:
    return tern<0xdc>(a, b, c, d);
  case 0xdd:
    return tern<0xdd>(a, b, c, d);
  case 0xde:
    return tern<0xde>(a, b, c, d);
  case 0xdf:
    return tern<0xdf>(a, b, c, d);
  case 0xe0:
    return tern<0xe0>(a, b, c, d);
  case 0xe1:
    return tern<0xe1>(a, b, c, d);
  case 0xe2:
    return tern<0xe2>(a, b, c, d);
  case 0xe3:
    return tern<0xe3>(a, b, c, d);
  case 0xe4:
    return tern<0xe4>(a, b, c, d);
  case 0xe5:
    return tern<0xe5>(a, b, c, d);
  case 0xe6:
    return tern<0xe6>(a, b, c, d);
  case 0xe7:
    return tern<0xe7>(a, b, c, d);
  case 0xe8:
    return tern<0xe8>(a, b, c, d);
  case 0xe9:
    return tern<0xe9>(a, b, c, d);
  case 0xea:
    return tern<0xea>(a, b, c, d);
  case 0xeb:
    return tern<0xeb>(a, b, c, d);
  case 0xec:
    return tern<0xec>(a, b, c, d);
  case 0xed:
    return tern<0xed>(a, b, c, d);
  case 0xee:
    return tern<0xee>(a, b, c, d);
  case 0xef:
    return tern<0xef>(a, b, c, d);
  case 0xf0:
    return tern<0xf0>(a, b, c, d);
  case 0xf1:
    return tern<0xf1>(a, b, c, d);
  case 0xf2:
    return tern<0xf2>(a, b, c, d);
  case 0xf3:
    return tern<0xf3>(a, b, c, d);
  case 0xf4:
    return tern<0xf4>(a, b, c, d);
  case 0xf5:
    return tern<0xf5>(a, b, c, d);
  case 0xf6:
    return tern<0xf6>(a, b, c, d);
  case 0xf7:
    return tern<0xf7>(a, b, c, d);
  case 0xf8:
    return tern<0xf8>(a, b, c, d);
  case 0xf9:
    return tern<0xf9>(a, b, c, d);
  case 0xfa:
    return tern<0xfa>(a, b, c, d);
  case 0xfb:
    return tern<0xfb>(a, b, c, d);
  case 0xfc:
    return tern<0xfc>(a, b, c, d);
  case 0xfd:
    return tern<0xfd>(a, b, c, d);
  case 0xfe:
    return tern<0xfe>(a, b, c, d);
  case 0xff:
    return tern<0xff>(a, b, c, d);
  default:
    __builtin_unreachable();
  }
}

__attribute__((noinline)) __m128i ternN_asm(__m128i a, __m128i b, __m128i c,
                                            __m128i d, uint8_t Imm) {
  switch (Imm) {
  case 0x0:
    return tern_asm<0x0>(a, b, c, d);
  case 0x1:
    return tern_asm<0x1>(a, b, c, d);
  case 0x2:
    return tern_asm<0x2>(a, b, c, d);
  case 0x3:
    return tern_asm<0x3>(a, b, c, d);
  case 0x4:
    return tern_asm<0x4>(a, b, c, d);
  case 0x5:
    return tern_asm<0x5>(a, b, c, d);
  case 0x6:
    return tern_asm<0x6>(a, b, c, d);
  case 0x7:
    return tern_asm<0x7>(a, b, c, d);
  case 0x8:
    return tern_asm<0x8>(a, b, c, d);
  case 0x9:
    return tern_asm<0x9>(a, b, c, d);
  case 0xa:
    return tern_asm<0xa>(a, b, c, d);
  case 0xb:
    return tern_asm<0xb>(a, b, c, d);
  case 0xc:
    return tern_asm<0xc>(a, b, c, d);
  case 0xd:
    return tern_asm<0xd>(a, b, c, d);
  case 0xe:
    return tern_asm<0xe>(a, b, c, d);
  case 0xf:
    return tern_asm<0xf>(a, b, c, d);
  case 0x10:
    return tern_asm<0x10>(a, b, c, d);
  case 0x11:
    return tern_asm<0x11>(a, b, c, d);
  case 0x12:
    return tern_asm<0x12>(a, b, c, d);
  case 0x13:
    return tern_asm<0x13>(a, b, c, d);
  case 0x14:
    return tern_asm<0x14>(a, b, c, d);
  case 0x15:
    return tern_asm<0x15>(a, b, c, d);
  case 0x16:
    return tern_asm<0x16>(a, b, c, d);
  case 0x17:
    return tern_asm<0x17>(a, b, c, d);
  case 0x18:
    return tern_asm<0x18>(a, b, c, d);
  case 0x19:
    return tern_asm<0x19>(a, b, c, d);
  case 0x1a:
    return tern_asm<0x1a>(a, b, c, d);
  case 0x1b:
    return tern_asm<0x1b>(a, b, c, d);
  case 0x1c:
    return tern_asm<0x1c>(a, b, c, d);
  case 0x1d:
    return tern_asm<0x1d>(a, b, c, d);
  case 0x1e:
    return tern_asm<0x1e>(a, b, c, d);
  case 0x1f:
    return tern_asm<0x1f>(a, b, c, d);
  case 0x20:
    return tern_asm<0x20>(a, b, c, d);
  case 0x21:
    return tern_asm<0x21>(a, b, c, d);
  case 0x22:
    return tern_asm<0x22>(a, b, c, d);
  case 0x23:
    return tern_asm<0x23>(a, b, c, d);
  case 0x24:
    return tern_asm<0x24>(a, b, c, d);
  case 0x25:
    return tern_asm<0x25>(a, b, c, d);
  case 0x26:
    return tern_asm<0x26>(a, b, c, d);
  case 0x27:
    return tern_asm<0x27>(a, b, c, d);
  case 0x28:
    return tern_asm<0x28>(a, b, c, d);
  case 0x29:
    return tern_asm<0x29>(a, b, c, d);
  case 0x2a:
    return tern_asm<0x2a>(a, b, c, d);
  case 0x2b:
    return tern_asm<0x2b>(a, b, c, d);
  case 0x2c:
    return tern_asm<0x2c>(a, b, c, d);
  case 0x2d:
    return tern_asm<0x2d>(a, b, c, d);
  case 0x2e:
    return tern_asm<0x2e>(a, b, c, d);
  case 0x2f:
    return tern_asm<0x2f>(a, b, c, d);
  case 0x30:
    return tern_asm<0x30>(a, b, c, d);
  case 0x31:
    return tern_asm<0x31>(a, b, c, d);
  case 0x32:
    return tern_asm<0x32>(a, b, c, d);
  case 0x33:
    return tern_asm<0x33>(a, b, c, d);
  case 0x34:
    return tern_asm<0x34>(a, b, c, d);
  case 0x35:
    return tern_asm<0x35>(a, b, c, d);
  case 0x36:
    return tern_asm<0x36>(a, b, c, d);
  case 0x37:
    return tern_asm<0x37>(a, b, c, d);
  case 0x38:
    return tern_asm<0x38>(a, b, c, d);
  case 0x39:
    return tern_asm<0x39>(a, b, c, d);
  case 0x3a:
    return tern_asm<0x3a>(a, b, c, d);
  case 0x3b:
    return tern_asm<0x3b>(a, b, c, d);
  case 0x3c:
    return tern_asm<0x3c>(a, b, c, d);
  case 0x3d:
    return tern_asm<0x3d>(a, b, c, d);
  case 0x3e:
    return tern_asm<0x3e>(a, b, c, d);
  case 0x3f:
    return tern_asm<0x3f>(a, b, c, d);
  case 0x40:
    return tern_asm<0x40>(a, b, c, d);
  case 0x41:
    return tern_asm<0x41>(a, b, c, d);
  case 0x42:
    return tern_asm<0x42>(a, b, c, d);
  case 0x43:
    return tern_asm<0x43>(a, b, c, d);
  case 0x44:
    return tern_asm<0x44>(a, b, c, d);
  case 0x45:
    return tern_asm<0x45>(a, b, c, d);
  case 0x46:
    return tern_asm<0x46>(a, b, c, d);
  case 0x47:
    return tern_asm<0x47>(a, b, c, d);
  case 0x48:
    return tern_asm<0x48>(a, b, c, d);
  case 0x49:
    return tern_asm<0x49>(a, b, c, d);
  case 0x4a:
    return tern_asm<0x4a>(a, b, c, d);
  case 0x4b:
    return tern_asm<0x4b>(a, b, c, d);
  case 0x4c:
    return tern_asm<0x4c>(a, b, c, d);
  case 0x4d:
    return tern_asm<0x4d>(a, b, c, d);
  case 0x4e:
    return tern_asm<0x4e>(a, b, c, d);
  case 0x4f:
    return tern_asm<0x4f>(a, b, c, d);
  case 0x50:
    return tern_asm<0x50>(a, b, c, d);
  case 0x51:
    return tern_asm<0x51>(a, b, c, d);
  case 0x52:
    return tern_asm<0x52>(a, b, c, d);
  case 0x53:
    return tern_asm<0x53>(a, b, c, d);
  case 0x54:
    return tern_asm<0x54>(a, b, c, d);
  case 0x55:
    return tern_asm<0x55>(a, b, c, d);
  case 0x56:
    return tern_asm<0x56>(a, b, c, d);
  case 0x57:
    return tern_asm<0x57>(a, b, c, d);
  case 0x58:
    return tern_asm<0x58>(a, b, c, d);
  case 0x59:
    return tern_asm<0x59>(a, b, c, d);
  case 0x5a:
    return tern_asm<0x5a>(a, b, c, d);
  case 0x5b:
    return tern_asm<0x5b>(a, b, c, d);
  case 0x5c:
    return tern_asm<0x5c>(a, b, c, d);
  case 0x5d:
    return tern_asm<0x5d>(a, b, c, d);
  case 0x5e:
    return tern_asm<0x5e>(a, b, c, d);
  case 0x5f:
    return tern_asm<0x5f>(a, b, c, d);
  case 0x60:
    return tern_asm<0x60>(a, b, c, d);
  case 0x61:
    return tern_asm<0x61>(a, b, c, d);
  case 0x62:
    return tern_asm<0x62>(a, b, c, d);
  case 0x63:
    return tern_asm<0x63>(a, b, c, d);
  case 0x64:
    return tern_asm<0x64>(a, b, c, d);
  case 0x65:
    return tern_asm<0x65>(a, b, c, d);
  case 0x66:
    return tern_asm<0x66>(a, b, c, d);
  case 0x67:
    return tern_asm<0x67>(a, b, c, d);
  case 0x68:
    return tern_asm<0x68>(a, b, c, d);
  case 0x69:
    return tern_asm<0x69>(a, b, c, d);
  case 0x6a:
    return tern_asm<0x6a>(a, b, c, d);
  case 0x6b:
    return tern_asm<0x6b>(a, b, c, d);
  case 0x6c:
    return tern_asm<0x6c>(a, b, c, d);
  case 0x6d:
    return tern_asm<0x6d>(a, b, c, d);
  case 0x6e:
    return tern_asm<0x6e>(a, b, c, d);
  case 0x6f:
    return tern_asm<0x6f>(a, b, c, d);
  case 0x70:
    return tern_asm<0x70>(a, b, c, d);
  case 0x71:
    return tern_asm<0x71>(a, b, c, d);
  case 0x72:
    return tern_asm<0x72>(a, b, c, d);
  case 0x73:
    return tern_asm<0x73>(a, b, c, d);
  case 0x74:
    return tern_asm<0x74>(a, b, c, d);
  case 0x75:
    return tern_asm<0x75>(a, b, c, d);
  case 0x76:
    return tern_asm<0x76>(a, b, c, d);
  case 0x77:
    return tern_asm<0x77>(a, b, c, d);
  case 0x78:
    return tern_asm<0x78>(a, b, c, d);
  case 0x79:
    return tern_asm<0x79>(a, b, c, d);
  case 0x7a:
    return tern_asm<0x7a>(a, b, c, d);
  case 0x7b:
    return tern_asm<0x7b>(a, b, c, d);
  case 0x7c:
    return tern_asm<0x7c>(a, b, c, d);
  case 0x7d:
    return tern_asm<0x7d>(a, b, c, d);
  case 0x7e:
    return tern_asm<0x7e>(a, b, c, d);
  case 0x7f:
    return tern_asm<0x7f>(a, b, c, d);
  case 0x80:
    return tern_asm<0x80>(a, b, c, d);
  case 0x81:
    return tern_asm<0x81>(a, b, c, d);
  case 0x82:
    return tern_asm<0x82>(a, b, c, d);
  case 0x83:
    return tern_asm<0x83>(a, b, c, d);
  case 0x84:
    return tern_asm<0x84>(a, b, c, d);
  case 0x85:
    return tern_asm<0x85>(a, b, c, d);
  case 0x86:
    return tern_asm<0x86>(a, b, c, d);
  case 0x87:
    return tern_asm<0x87>(a, b, c, d);
  case 0x88:
    return tern_asm<0x88>(a, b, c, d);
  case 0x89:
    return tern_asm<0x89>(a, b, c, d);
  case 0x8a:
    return tern_asm<0x8a>(a, b, c, d);
  case 0x8b:
    return tern_asm<0x8b>(a, b, c, d);
  case 0x8c:
    return tern_asm<0x8c>(a, b, c, d);
  case 0x8d:
    return tern_asm<0x8d>(a, b, c, d);
  case 0x8e:
    return tern_asm<0x8e>(a, b, c, d);
  case 0x8f:
    return tern_asm<0x8f>(a, b, c, d);
  case 0x90:
    return tern_asm<0x90>(a, b, c, d);
  case 0x91:
    return tern_asm<0x91>(a, b, c, d);
  case 0x92:
    return tern_asm<0x92>(a, b, c, d);
  case 0x93:
    return tern_asm<0x93>(a, b, c, d);
  case 0x94:
    return tern_asm<0x94>(a, b, c, d);
  case 0x95:
    return tern_asm<0x95>(a, b, c, d);
  case 0x96:
    return tern_asm<0x96>(a, b, c, d);
  case 0x97:
    return tern_asm<0x97>(a, b, c, d);
  case 0x98:
    return tern_asm<0x98>(a, b, c, d);
  case 0x99:
    return tern_asm<0x99>(a, b, c, d);
  case 0x9a:
    return tern_asm<0x9a>(a, b, c, d);
  case 0x9b:
    return tern_asm<0x9b>(a, b, c, d);
  case 0x9c:
    return tern_asm<0x9c>(a, b, c, d);
  case 0x9d:
    return tern_asm<0x9d>(a, b, c, d);
  case 0x9e:
    return tern_asm<0x9e>(a, b, c, d);
  case 0x9f:
    return tern_asm<0x9f>(a, b, c, d);
  case 0xa0:
    return tern_asm<0xa0>(a, b, c, d);
  case 0xa1:
    return tern_asm<0xa1>(a, b, c, d);
  case 0xa2:
    return tern_asm<0xa2>(a, b, c, d);
  case 0xa3:
    return tern_asm<0xa3>(a, b, c, d);
  case 0xa4:
    return tern_asm<0xa4>(a, b, c, d);
  case 0xa5:
    return tern_asm<0xa5>(a, b, c, d);
  case 0xa6:
    return tern_asm<0xa6>(a, b, c, d);
  case 0xa7:
    return tern_asm<0xa7>(a, b, c, d);
  case 0xa8:
    return tern_asm<0xa8>(a, b, c, d);
  case 0xa9:
    return tern_asm<0xa9>(a, b, c, d);
  case 0xaa:
    return tern_asm<0xaa>(a, b, c, d);
  case 0xab:
    return tern_asm<0xab>(a, b, c, d);
  case 0xac:
    return tern_asm<0xac>(a, b, c, d);
  case 0xad:
    return tern_asm<0xad>(a, b, c, d);
  case 0xae:
    return tern_asm<0xae>(a, b, c, d);
  case 0xaf:
    return tern_asm<0xaf>(a, b, c, d);
  case 0xb0:
    return tern_asm<0xb0>(a, b, c, d);
  case 0xb1:
    return tern_asm<0xb1>(a, b, c, d);
  case 0xb2:
    return tern_asm<0xb2>(a, b, c, d);
  case 0xb3:
    return tern_asm<0xb3>(a, b, c, d);
  case 0xb4:
    return tern_asm<0xb4>(a, b, c, d);
  case 0xb5:
    return tern_asm<0xb5>(a, b, c, d);
  case 0xb6:
    return tern_asm<0xb6>(a, b, c, d);
  case 0xb7:
    return tern_asm<0xb7>(a, b, c, d);
  case 0xb8:
    return tern_asm<0xb8>(a, b, c, d);
  case 0xb9:
    return tern_asm<0xb9>(a, b, c, d);
  case 0xba:
    return tern_asm<0xba>(a, b, c, d);
  case 0xbb:
    return tern_asm<0xbb>(a, b, c, d);
  case 0xbc:
    return tern_asm<0xbc>(a, b, c, d);
  case 0xbd:
    return tern_asm<0xbd>(a, b, c, d);
  case 0xbe:
    return tern_asm<0xbe>(a, b, c, d);
  case 0xbf:
    return tern_asm<0xbf>(a, b, c, d);
  case 0xc0:
    return tern_asm<0xc0>(a, b, c, d);
  case 0xc1:
    return tern_asm<0xc1>(a, b, c, d);
  case 0xc2:
    return tern_asm<0xc2>(a, b, c, d);
  case 0xc3:
    return tern_asm<0xc3>(a, b, c, d);
  case 0xc4:
    return tern_asm<0xc4>(a, b, c, d);
  case 0xc5:
    return tern_asm<0xc5>(a, b, c, d);
  case 0xc6:
    return tern_asm<0xc6>(a, b, c, d);
  case 0xc7:
    return tern_asm<0xc7>(a, b, c, d);
  case 0xc8:
    return tern_asm<0xc8>(a, b, c, d);
  case 0xc9:
    return tern_asm<0xc9>(a, b, c, d);
  case 0xca:
    return tern_asm<0xca>(a, b, c, d);
  case 0xcb:
    return tern_asm<0xcb>(a, b, c, d);
  case 0xcc:
    return tern_asm<0xcc>(a, b, c, d);
  case 0xcd:
    return tern_asm<0xcd>(a, b, c, d);
  case 0xce:
    return tern_asm<0xce>(a, b, c, d);
  case 0xcf:
    return tern_asm<0xcf>(a, b, c, d);
  case 0xd0:
    return tern_asm<0xd0>(a, b, c, d);
  case 0xd1:
    return tern_asm<0xd1>(a, b, c, d);
  case 0xd2:
    return tern_asm<0xd2>(a, b, c, d);
  case 0xd3:
    return tern_asm<0xd3>(a, b, c, d);
  case 0xd4:
    return tern_asm<0xd4>(a, b, c, d);
  case 0xd5:
    return tern_asm<0xd5>(a, b, c, d);
  case 0xd6:
    return tern_asm<0xd6>(a, b, c, d);
  case 0xd7:
    return tern_asm<0xd7>(a, b, c, d);
  case 0xd8:
    return tern_asm<0xd8>(a, b, c, d);
  case 0xd9:
    return tern_asm<0xd9>(a, b, c, d);
  case 0xda:
    return tern_asm<0xda>(a, b, c, d);
  case 0xdb:
    return tern_asm<0xdb>(a, b, c, d);
  case 0xdc:
    return tern_asm<0xdc>(a, b, c, d);
  case 0xdd:
    return tern_asm<0xdd>(a, b, c, d);
  case 0xde:
    return tern_asm<0xde>(a, b, c, d);
  case 0xdf:
    return tern_asm<0xdf>(a, b, c, d);
  case 0xe0:
    return tern_asm<0xe0>(a, b, c, d);
  case 0xe1:
    return tern_asm<0xe1>(a, b, c, d);
  case 0xe2:
    return tern_asm<0xe2>(a, b, c, d);
  case 0xe3:
    return tern_asm<0xe3>(a, b, c, d);
  case 0xe4:
    return tern_asm<0xe4>(a, b, c, d);
  case 0xe5:
    return tern_asm<0xe5>(a, b, c, d);
  case 0xe6:
    return tern_asm<0xe6>(a, b, c, d);
  case 0xe7:
    return tern_asm<0xe7>(a, b, c, d);
  case 0xe8:
    return tern_asm<0xe8>(a, b, c, d);
  case 0xe9:
    return tern_asm<0xe9>(a, b, c, d);
  case 0xea:
    return tern_asm<0xea>(a, b, c, d);
  case 0xeb:
    return tern_asm<0xeb>(a, b, c, d);
  case 0xec:
    return tern_asm<0xec>(a, b, c, d);
  case 0xed:
    return tern_asm<0xed>(a, b, c, d);
  case 0xee:
    return tern_asm<0xee>(a, b, c, d);
  case 0xef:
    return tern_asm<0xef>(a, b, c, d);
  case 0xf0:
    return tern_asm<0xf0>(a, b, c, d);
  case 0xf1:
    return tern_asm<0xf1>(a, b, c, d);
  case 0xf2:
    return tern_asm<0xf2>(a, b, c, d);
  case 0xf3:
    return tern_asm<0xf3>(a, b, c, d);
  case 0xf4:
    return tern_asm<0xf4>(a, b, c, d);
  case 0xf5:
    return tern_asm<0xf5>(a, b, c, d);
  case 0xf6:
    return tern_asm<0xf6>(a, b, c, d);
  case 0xf7:
    return tern_asm<0xf7>(a, b, c, d);
  case 0xf8:
    return tern_asm<0xf8>(a, b, c, d);
  case 0xf9:
    return tern_asm<0xf9>(a, b, c, d);
  case 0xfa:
    return tern_asm<0xfa>(a, b, c, d);
  case 0xfb:
    return tern_asm<0xfb>(a, b, c, d);
  case 0xfc:
    return tern_asm<0xfc>(a, b, c, d);
  case 0xfd:
    return tern_asm<0xfd>(a, b, c, d);
  case 0xfe:
    return tern_asm<0xfe>(a, b, c, d);
  case 0xff:
    return tern_asm<0xff>(a, b, c, d);
  default:
    __builtin_unreachable();
  }
}

static void randomize_buf(uint8_t *p, uint64_t sz) {
  int64_t ret = getrandom(p, sz, 0);
  assert(ret > 0 && ((uint64_t)ret) == sz);
}

static uint8_t *random_buf(uint64_t sz) {
  uint8_t *p = (uint8_t *)malloc(sz);
  assert(p);
  randomize_buf(p, sz);
  return p;
}

int main() {
  enum { K_sz = 1 << 20, K_off = 4 * sizeof(__m128i) };
  uint8_t *p = random_buf(K_sz);
  uint32_t i;
  for (;;) {
    for (i = 0; i < K_sz; i += K_off) {
      __m128i vecs[4];
      __m128i new_r, ref_r;
      __builtin_memcpy(&vecs, p + i, K_off);
      for (uint32_t imm = 0; imm < 256; ++imm) {
        ref_r = ternN(vecs[0], vecs[1], vecs[2], vecs[3], imm);
        new_r = ternN_asm(vecs[0], vecs[1], vecs[2], vecs[3], imm);
        assert(!__builtin_memcmp(&ref_r, &new_r, sizeof(__m128i)));
      }
    }
    randomize_buf(p, K_sz);
  }
}