MirrorHub/construct
0
0
Fork 0
mirror of https://github.com/matrix-construct/construct synced 2024-06-11 06:28:55 +02:00
Code Issues Releases Wiki Activity

ircd::utf: Eliminate recasting for shift.

Browse source
This commit is contained in:
Jason Volk 2020-07-08 17:26:48 -07:00
parent e730c1a0bb
commit 2f9aa15fc0
3 changed files with 21 additions and 21 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

8
include/ircd/simd/shift.h
View file

@ -48,7 +48,7 @@ noexcept
b % 8 == 0, "xmmx register only shifts right at bytewise resolution."
);
return _mm_bsrli_si128(a, b / 8);
return T(_mm_bsrli_si128(u128x1(a), b / 8));
}
#endif
@ -65,7 +65,7 @@ noexcept
b % 8 == 0, "xmmx register only shifts left at bytewise resolution."
);
return _mm_bslli_si128(a, b / 8);
return T(_mm_bslli_si128(u128x1(a), b / 8));
}
#endif
@ -82,7 +82,7 @@ noexcept
b % 8 == 0, "ymmx register only shifts right at bytewise resolution."
);
return _mm256_srli_si256(a, b / 8);
return T(_mm256_srli_si256(u256x1(a), b / 8));
}
#endif
@ -99,6 +99,6 @@ noexcept
b % 8 == 0, "ymmx register only shifts left at bytewise resolution."
);
return _mm256_slli_si256(a, b / 8);
return T(_mm256_slli_si256(u256x1(a), b / 8));
}
#endif

12
include/ircd/utf.h
View file

@ -57,13 +57,13 @@ inline ircd::u8x16
ircd::utf16::mask_surrogate(const u8x16 found)
noexcept
{
return u128x1
return u8x16
{
shl<0x08>(u128x1(found)) |
shl<0x10>(u128x1(found)) |
shl<0x18>(u128x1(found)) |
shl<0x20>(u128x1(found)) |
shl<0x28>(u128x1(found)) |
shl<0x08>(found) |
shl<0x10>(found) |
shl<0x18>(found) |
shl<0x20>(found) |
shl<0x28>(found) |
found
};
}

22
ircd/utf.cc
View file

@ -43,8 +43,8 @@ noexcept
// Masks the starting byte (the '\' char) of each valid surrogate.
const u32x4 is_surrogate
{
u128x1(input == '\\') &
shr<8>(u128x1(input == 'u')) &
(input == '\\') &
shr<8>(input == 'u') &
shr<16>(is_hex_nibble) &
shr<24>(is_hex_nibble) &
shr<32>(is_hex_nibble) &
@ -64,20 +64,20 @@ noexcept
// between both lanes if so.
const u32x4 surrogate_deuce
{
(surrogate_mask & shr<32>(u128x1(surrogate_mask))) |
(surrogate_mask & shl<32>(u128x1(surrogate_mask)))
(surrogate_mask & shr<32>(surrogate_mask)) |
(surrogate_mask & shl<32>(surrogate_mask))
};
// ASCII to integral converion of the upper nibbles
const u8x16 hex_upper
{
shr<16>(u128x1(hex_nibble))
shr<16>(hex_nibble)
};
// ASCII to integral converion of the lower nibbles
const u8x16 hex_lower
{
shr<24>(u128x1(hex_nibble))
shr<24>(hex_nibble)
};
// pack upper and lower nibbles into bytes, though these have a space
@ -108,13 +108,13 @@ noexcept
// Mask lane[0] if the codepoints are actually a surrogate pair
const u32x4 surrogate_paired
{
surrogate_pair_range & shr<32>(u128x1(surrogate_pair_range))
surrogate_pair_range & shr<32>(surrogate_pair_range)
};
// Pre-processing shuffle for surrogate pair decode
const u32x4 codepoint_pre_paired
{
shr<16>(u128x1(codepoint_unpaired)) | codepoint_unpaired
shr<16>(codepoint_unpaired) | codepoint_unpaired
};
// Decode surrogate pair
@ -134,7 +134,7 @@ noexcept
// Decide if the codepoint is in the BMP (2- bytes)
const u32x4 codepoint_low
{
(codepoint_paired <= 0xffffU) & ~(shl<32>(u128x1(codepoint_high)))
(codepoint_paired <= 0xffffU) & ~(shl<32>(codepoint_high))
};
// When two surrogates in a pair are input, lane[0] only
@ -260,8 +260,8 @@ noexcept
const auto is_surrogate
{
u128x1(input == '\\') &
shr<8>(u128x1(input == 'u')) &
(input == '\\') &
shr<8>(input == 'u') &
shr<16>(is_hex_nibble) &
shr<24>(is_hex_nibble) &
shr<32>(is_hex_nibble) &