memx 0.2.0

memory functions like libc memcmp(), memchr(), memmem(), memcpy(), memset()
Documentation 
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54

// multiplicative
pub(crate) mod dbl;
pub(crate) mod qpl;
pub(crate) mod sgl;
pub(crate) mod tpl;

#[cfg(target_arch = "x86")]
use core::arch::x86 as mmx;
#[cfg(target_arch = "x86_64")]
use core::arch::x86_64 as mmx;

use mmx::__m128i;
use mmx::_mm_cmpeq_epi8;
use mmx::_mm_movemask_epi8;
use mmx::_mm_set1_epi8;

use mmx::__m256i;
use mmx::_mm256_cmpeq_epi8;
use mmx::_mm256_cvtsi256_si32;
use mmx::_mm256_movemask_epi8;
use mmx::_mm256_set1_epi8;

#[inline(always)]
unsafe fn _b16_value(c: u8) -> __m128i {
    unsafe { _mm_set1_epi8(c as i8) }
}

#[inline(always)]
unsafe fn _b32_value(c: u8) -> __m256i {
    unsafe { _mm256_set1_epi8(c as i8) }
}

#[inline(always)]
unsafe fn _b16_from_b32(cc: __m256i) -> __m128i {
    unsafe { _b16_value(_mm256_cvtsi256_si32(cc) as u8) }
}

#[inline(always)]
unsafe fn _b16_eq(mm_a: __m128i, mm_b: __m128i) -> bool {
    unsafe {
        let mm_eq = _mm_cmpeq_epi8(mm_a, mm_b);
        let mask = _mm_movemask_epi8(mm_eq);
        mask == 0xFFFF
    }
}

#[inline(always)]
unsafe fn _b32_eq(mm_a: __m256i, mm_b: __m256i) -> bool {
    unsafe {
        let mm_eq = _mm256_cmpeq_epi8(mm_a, mm_b);
        let mask = _mm256_movemask_epi8(mm_eq) as u32;
        mask == 0xFFFF_FFFF
    }
}