use crate::{mem, static_cast_i8};
#[cfg(target_arch = "x86")]
use std::arch::x86::{
__m256i, _mm256_add_epi8, _mm256_alignr_epi8, _mm256_and_si256, _mm256_cmpeq_epi8,
_mm256_cmpgt_epi8, _mm256_or_si256, _mm256_permute2x128_si256, _mm256_set1_epi8,
_mm256_setr_epi8, _mm256_setzero_si256, _mm256_shuffle_epi8, _mm256_srli_epi16,
_mm256_subs_epu8,
};
#[cfg(target_arch = "x86_64")]
use std::arch::x86_64::{
__m256i, _mm256_add_epi8, _mm256_alignr_epi8, _mm256_and_si256, _mm256_cmpeq_epi8,
_mm256_cmpgt_epi8, _mm256_or_si256, _mm256_permute2x128_si256, _mm256_set1_epi8,
_mm256_setr_epi8, _mm256_setzero_si256, _mm256_shuffle_epi8, _mm256_srli_epi16,
_mm256_subs_epu8,
};
use crate::utf8check::{ProcessedUtfBytes, Utf8Check};
macro_rules! initial_mins {
() => {
_mm256_setr_epi8(
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128, static_cast_i8!(0xC2_u8),
-128, static_cast_i8!(0xE1_u8), static_cast_i8!(0xF1_u8), -128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128, static_cast_i8!(0xC2_u8),
-128, static_cast_i8!(0xE1_u8), static_cast_i8!(0xF1_u8), )
};
}
macro_rules! second_mins {
() => {
_mm256_setr_epi8(
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128, 127,
127, static_cast_i8!(0xA0_u8), static_cast_i8!(0x90_u8), -128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128,
-128, 127,
127, static_cast_i8!(0xA0_u8), static_cast_i8!(0x90_u8), )
};
}
impl Default for ProcessedUtfBytes<__m256i> {
#[cfg_attr(not(feature = "no-inline"), inline)]
fn default() -> Self {
unsafe {
Self {
rawbytes: _mm256_setzero_si256(),
high_nibbles: _mm256_setzero_si256(),
carried_continuations: _mm256_setzero_si256(),
}
}
}
}
impl Utf8Check<__m256i> for ProcessedUtfBytes<__m256i> {
#[cfg_attr(not(feature = "no-inline"), inline(always))]
fn new_processed_utf_bytes() -> Self {
Self::default()
}
#[cfg_attr(not(feature = "no-inline"), inline)]
fn push_last_byte_of_a_to_b(a: __m256i, b: __m256i) -> __m256i {
unsafe { _mm256_alignr_epi8(b, _mm256_permute2x128_si256(a, b, 0x21), 15) }
}
#[cfg_attr(not(feature = "no-inline"), inline)]
fn push_last_2bytes_of_a_to_b(a: __m256i, b: __m256i) -> __m256i {
unsafe { _mm256_alignr_epi8(b, _mm256_permute2x128_si256(a, b, 0x21), 14) }
}
#[cfg_attr(not(feature = "no-inline"), inline)]
fn check_smaller_than_0xf4(current_bytes: __m256i, has_error: &mut __m256i) {
*has_error = unsafe {
_mm256_or_si256(
*has_error,
_mm256_subs_epu8(current_bytes, _mm256_set1_epi8(static_cast_i8!(0xF4_u8))),
)
};
}
#[cfg_attr(not(feature = "no-inline"), inline)]
fn continuation_lengths(high_nibbles: __m256i) -> __m256i {
unsafe {
_mm256_shuffle_epi8(
_mm256_setr_epi8(
1, 1, 1, 1, 1, 1, 1, 1, 0, 0, 0, 0, 2, 2, 3, 4, 1, 1, 1, 1, 1, 1, 1, 1, 0, 0, 0, 0, 2, 2, 3, 4, ),
high_nibbles,
)
}
}
#[cfg_attr(not(feature = "no-inline"), inline)]
fn carry_continuations(initial_lengths: __m256i, previous_carries: __m256i) -> __m256i {
unsafe {
let right1: __m256i = _mm256_subs_epu8(
Self::push_last_byte_of_a_to_b(previous_carries, initial_lengths),
_mm256_set1_epi8(1),
);
let sum: __m256i = _mm256_add_epi8(initial_lengths, right1);
let right2: __m256i = _mm256_subs_epu8(
Self::push_last_2bytes_of_a_to_b(previous_carries, sum),
_mm256_set1_epi8(2),
);
_mm256_add_epi8(sum, right2)
}
}
#[cfg_attr(not(feature = "no-inline"), inline)]
fn check_continuations(initial_lengths: __m256i, carries: __m256i, has_error: &mut __m256i) {
unsafe {
let overunder: __m256i = _mm256_cmpeq_epi8(
_mm256_cmpgt_epi8(carries, initial_lengths),
_mm256_cmpgt_epi8(initial_lengths, _mm256_setzero_si256()),
);
*has_error = _mm256_or_si256(*has_error, overunder);
}
}
#[cfg_attr(not(feature = "no-inline"), inline)]
fn check_first_continuation_max(
current_bytes: __m256i,
off1_current_bytes: __m256i,
has_error: &mut __m256i,
) {
unsafe {
let mask_ed: __m256i = _mm256_cmpeq_epi8(
off1_current_bytes,
_mm256_set1_epi8(static_cast_i8!(0xED_u8)),
);
let mask_f4: __m256i = _mm256_cmpeq_epi8(
off1_current_bytes,
_mm256_set1_epi8(static_cast_i8!(0xF4_u8)),
);
let badfollow_ed: __m256i = _mm256_and_si256(
_mm256_cmpgt_epi8(current_bytes, _mm256_set1_epi8(static_cast_i8!(0x9F_u8))),
mask_ed,
);
let badfollow_f4: __m256i = _mm256_and_si256(
_mm256_cmpgt_epi8(current_bytes, _mm256_set1_epi8(static_cast_i8!(0x8F_u8))),
mask_f4,
);
*has_error = _mm256_or_si256(*has_error, _mm256_or_si256(badfollow_ed, badfollow_f4));
}
}
#[cfg_attr(not(feature = "no-inline"), inline)]
fn check_overlong(
current_bytes: __m256i,
off1_current_bytes: __m256i,
hibits: __m256i,
previous_hibits: __m256i,
has_error: &mut __m256i,
) {
unsafe {
let off1_hibits: __m256i = Self::push_last_byte_of_a_to_b(previous_hibits, hibits);
let initial_mins: __m256i = _mm256_shuffle_epi8(initial_mins!(), off1_hibits);
let initial_under: __m256i = _mm256_cmpgt_epi8(initial_mins, off1_current_bytes);
let second_mins: __m256i = _mm256_shuffle_epi8(second_mins!(), off1_hibits);
let second_under: __m256i = _mm256_cmpgt_epi8(second_mins, current_bytes);
*has_error = _mm256_or_si256(*has_error, _mm256_and_si256(initial_under, second_under));
}
}
#[cfg_attr(not(feature = "no-inline"), inline)]
fn count_nibbles(bytes: __m256i, answer: &mut Self) {
answer.rawbytes = bytes;
answer.high_nibbles =
unsafe { _mm256_and_si256(_mm256_srli_epi16(bytes, 4), _mm256_set1_epi8(0x0F)) };
}
}