Struct vectoreyes::U64x4

source · [−]

#[repr(transparent)]
pub struct U64x4(_);

Expand description

[u64; 4] as a vector.

Implementations

source

impl U64x4

source

pub const fn from_array(array: [u64 ; 4]) -> U64x4

Create a vector from an array.

Unlike the From trait function, the from_array function is const.

Example

const MY_EXTREMELY_FUN_VALUE: U64x4 =
    U64x4::from_array([0, 1, 2, 3]);
for (i, value) in MY_EXTREMELY_FUN_VALUE.as_array().iter().copied().enumerate() {
    assert_eq!(i as u64, value);
}

Avx2

Trait Implementations

source

impl Add<U64x4> for U64x4

source

fn add(self, rhs: U64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    self.as_array()[0].wrapping_add(rhs.as_array()[0]),
    self.as_array()[1].wrapping_add(rhs.as_array()[1]),
    self.as_array()[2].wrapping_add(rhs.as_array()[2]),
    self.as_array()[3].wrapping_add(rhs.as_array()[3]),
])

Avx2

_mm256_add_epi64
- VPADDQ ymm, ymm, ymm

type Output = U64x4

The resulting type after applying the + operator.

source

impl AddAssign<U64x4> for U64x4

source

fn add_assign(&mut self, rhs: Self)

Performs the += operation. Read more

source

impl BitAnd<U64x4> for U64x4

source

fn bitand(self, rhs: U64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    self.as_array()[0] & rhs.as_array()[0],
    self.as_array()[1] & rhs.as_array()[1],
    self.as_array()[2] & rhs.as_array()[2],
    self.as_array()[3] & rhs.as_array()[3],
])

Avx2

_mm256_and_si256
- VPAND ymm, ymm, ymm

type Output = U64x4

The resulting type after applying the & operator.

source

impl BitAndAssign<U64x4> for U64x4

source

fn bitand_assign(&mut self, rhs: Self)

Performs the &= operation. Read more

source

impl BitOr<U64x4> for U64x4

source

fn bitor(self, rhs: U64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    self.as_array()[0] | rhs.as_array()[0],
    self.as_array()[1] | rhs.as_array()[1],
    self.as_array()[2] | rhs.as_array()[2],
    self.as_array()[3] | rhs.as_array()[3],
])

Avx2

_mm256_or_si256
- VPOR ymm, ymm, ymm

type Output = U64x4

The resulting type after applying the | operator.

source

impl BitOrAssign<U64x4> for U64x4

source

fn bitor_assign(&mut self, rhs: Self)

Performs the |= operation. Read more

source

impl BitXor<U64x4> for U64x4

source

fn bitxor(self, rhs: U64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    self.as_array()[0] ^ rhs.as_array()[0],
    self.as_array()[1] ^ rhs.as_array()[1],
    self.as_array()[2] ^ rhs.as_array()[2],
    self.as_array()[3] ^ rhs.as_array()[3],
])

Avx2

_mm256_xor_si256
- VPXOR ymm, ymm, ymm

type Output = U64x4

The resulting type after applying the ^ operator.

source

impl BitXorAssign<U64x4> for U64x4

source

fn bitxor_assign(&mut self, rhs: Self)

Performs the ^= operation. Read more

source

impl Clone for U64x4

source

fn clone(&self) -> U64x4

Returns a copy of the value. Read more

1.0.0 · source

fn clone_from(&mut self, source: &Self)

Performs copy-assignment from source. Read more

source

impl ConditionallySelectable for U64x4

source

fn conditional_select(a: &Self, b: &Self, choice: Choice) -> Self

Select a or b according to choice. Read more

source

fn conditional_assign(&mut self, other: &Self, choice: Choice)

Conditionally assign other to self, according to choice. Read more

source

fn conditional_swap(a: &mut Self, b: &mut Self, choice: Choice)

Conditionally swap self and other if choice == 1; otherwise, reassign both unto themselves. Read more

source

impl ConstantTimeEq for U64x4

source

fn ct_eq(&self, other: &Self) -> Choice

Determine if two items are equal. Read more

source

impl Debug for U64x4

source

fn fmt(&self, f: &mut Formatter<'_>) -> Result

Formats the value using the given formatter. Read more

source

impl Default for U64x4

source

fn default() -> Self

The zero vector.

source

impl ExtendingCast<U16x8> for U64x4

source

fn extending_cast_from(vector: U16x8) -> U64x4

Scalar Equivalent:

U64x4::from([
        u64::from(vector.as_array()[0]),
        u64::from(vector.as_array()[1]),
        u64::from(vector.as_array()[2]),
        u64::from(vector.as_array()[3]),
])

Avx2

_mm256_cvtepu16_epi64
- VPMOVZXWQ ymm, xmm

source

impl ExtendingCast<U32x4> for U64x4

source

fn extending_cast_from(vector: U32x4) -> U64x4

Scalar Equivalent:

U64x4::from([
        u64::from(vector.as_array()[0]),
        u64::from(vector.as_array()[1]),
        u64::from(vector.as_array()[2]),
        u64::from(vector.as_array()[3]),
])

Avx2

_mm256_cvtepu32_epi64
- VPMOVZXDQ ymm, xmm

source

impl ExtendingCast<U8x16> for U64x4

source

fn extending_cast_from(vector: U8x16) -> U64x4

Scalar Equivalent:

U64x4::from([
        u64::from(vector.as_array()[0]),
        u64::from(vector.as_array()[1]),
        u64::from(vector.as_array()[2]),
        u64::from(vector.as_array()[3]),
])

Avx2

_mm256_cvtepu8_epi64
- VPMOVZXBQ ymm, xmm

source

impl From<[U64x2 ; 2]> for U64x4

source

fn from(vectors: [U64x2 ; 2]) -> U64x4

Scalar Equivalent:

let mut out = [0; 4];
out[0..2].copy_from_slice(&vectors[0].as_array());
out[2..].copy_from_slice(&vectors[1].as_array());
U64x4::from(out)

Avx2

_mm256_set_m128i
- VINSERTF128 ymm, ymm, xmm, imm8

source

impl From<[u64 ; 4]> for U64x4

source

fn from(array: [u64 ; 4]) -> U64x4

Avx2

_mm256_loadu_si256
- VMOVDQU ymm, m256

source

impl From<I16x16> for U64x4

source

fn from(x: I16x16) -> U64x4

This cast is 100% free. It reinterprets the little-endinan bits of I16x16 as little endian bits of U64x4.

source

impl From<I32x8> for U64x4

source

fn from(x: I32x8) -> U64x4

This cast is 100% free. It reinterprets the little-endinan bits of I32x8 as little endian bits of U64x4.

source

impl From<I64x4> for U64x4

source

fn from(x: I64x4) -> U64x4

This cast is 100% free. It reinterprets the little-endinan bits of I64x4 as little endian bits of U64x4.

source

impl From<I8x32> for U64x4

source

fn from(x: I8x32) -> U64x4

This cast is 100% free. It reinterprets the little-endinan bits of I8x32 as little endian bits of U64x4.

source

impl From<U16x16> for U64x4

source

fn from(x: U16x16) -> U64x4

This cast is 100% free. It reinterprets the little-endinan bits of U16x16 as little endian bits of U64x4.

source

impl From<U32x4> for U64x4

source

fn from(vector: U32x4) -> U64x4

Scalar Equivalent:

U64x4::from([
        u64::from(vector.as_array()[0]),
        u64::from(vector.as_array()[1]),
        u64::from(vector.as_array()[2]),
        u64::from(vector.as_array()[3]),
])

Avx2

_mm256_cvtepu32_epi64
- VPMOVZXDQ ymm, xmm

source

impl From<U32x8> for U64x4

source

fn from(x: U32x8) -> U64x4

This cast is 100% free. It reinterprets the little-endinan bits of U32x8 as little endian bits of U64x4.

source

impl From<U64x2> for U64x4

source

fn from(vector: U64x2) -> U64x4

NOTE: this will zero the upper bits of the destination. Other intrinsics are more effcient, but leave the upper bits undefined. At present, these more effcient intrinsics are not exposed.

Scalar Equivalent:

let mut out = [0; 4];
out[0..2].copy_from_slice(&vector.as_array());
U64x4::from(out)

Avx2

_mm256_zextsi128_si256

source

impl From<U64x4> for [U64x2 ; 2]

source

fn from(vector: U64x4) -> [U64x2 ; 2]

Scalar Equivalent:

let mut lo = [0; 2];
let mut hi = [0; 2];
lo.copy_from_slice(&vector.as_array()[0..2]);
hi.copy_from_slice(&vector.as_array()[2..]);
[U64x2::from(lo), U64x2::from(hi)]

Avx2

_mm256_extracti128_si256
- VEXTRACTI128 xmm, ymm, imm8

source

impl From<U64x4> for [u64 ; 4]

source

fn from(vector: U64x4) -> [u64 ; 4]

Avx2

_mm256_storeu_si256
- VMOVDQU m256, ymm

source

impl From<U64x4> for I16x16

source

fn from(x: U64x4) -> I16x16

This cast is 100% free. It reinterprets the little-endinan bits of U64x4 as little endian bits of I16x16.

source

impl From<U64x4> for I32x8

source

fn from(x: U64x4) -> I32x8

This cast is 100% free. It reinterprets the little-endinan bits of U64x4 as little endian bits of I32x8.

source

impl From<U64x4> for I64x4

source

fn from(x: U64x4) -> I64x4

This cast is 100% free. It reinterprets the little-endinan bits of U64x4 as little endian bits of I64x4.

source

impl From<U64x4> for I8x32

source

fn from(x: U64x4) -> I8x32

This cast is 100% free. It reinterprets the little-endinan bits of U64x4 as little endian bits of I8x32.

source

impl From<U64x4> for U16x16

source

fn from(x: U64x4) -> U16x16

This cast is 100% free. It reinterprets the little-endinan bits of U64x4 as little endian bits of U16x16.

source

impl From<U64x4> for U32x8

source

fn from(x: U64x4) -> U32x8

This cast is 100% free. It reinterprets the little-endinan bits of U64x4 as little endian bits of U32x8.

source

impl From<U64x4> for U8x32

source

fn from(x: U64x4) -> U8x32

This cast is 100% free. It reinterprets the little-endinan bits of U64x4 as little endian bits of U8x32.

source

impl From<U8x32> for U64x4

source

fn from(x: U8x32) -> U64x4

This cast is 100% free. It reinterprets the little-endinan bits of U8x32 as little endian bits of U64x4.

source

impl Hash for U64x4

source

fn hash<H: Hasher>(&self, state: &mut H)

Feeds this value into the given Hasher. Read more

1.3.0 · source

fn hash_slice<H>(data: &[Self], state: &mut H)where
H: Hasher,

Feeds a slice of this type into the given Hasher. Read more

source

impl PartialEq<U64x4> for U64x4

source

fn eq(&self, other: &Self) -> bool

This method tests for self and other values to be equal, and is used by ==. Read more

1.0.0 · source

fn ne(&self, other: &Rhs) -> bool

This method tests for !=. The default implementation is almost always sufficient, and should not be overridden without very good reason. Read more

source

impl Shl<U64x4> for U64x4

source

fn shl(self, amount: U64x4) -> U64x4

Scalar Equivalent:

let mut out = self.as_array();
for (x, amm) in out.iter_mut().zip(amount.as_array().iter().copied()) {
    *x = if amm >= 64  {
        0
    } else {
        *x << amm
    };
}
U64x4::from(out)

Avx2

_mm256_sllv_epi64
- VPSLLVQ ymm, ymm, ymm

type Output = U64x4

The resulting type after applying the << operator.

source

impl Shl<u64> for U64x4

source

fn shl(self, amount: u64) -> U64x4

Scalar Equivalent:

if amount >= 64 {
    U64x4::ZERO
} else {
    U64x4::from([
        self.as_array()[0] << amount,
        self.as_array()[1] << amount,
        self.as_array()[2] << amount,
        self.as_array()[3] << amount,
    ])
}

Avx2

_mm256_sll_epi64
- VPSLLQ ymm, ymm, xmm
_mm_set_epi64x

Instruction sequence.

type Output = U64x4

The resulting type after applying the << operator.

source

impl ShlAssign<U64x4> for U64x4

source

fn shl_assign(&mut self, amount: U64x4)

Performs the <<= operation. Read more

source

impl ShlAssign<u64> for U64x4

source

fn shl_assign(&mut self, amount: u64)

Performs the <<= operation. Read more

source

impl Shr<U64x4> for U64x4

source

fn shr(self, amount: U64x4) -> U64x4

Scalar Equivalent:

let mut out = self.as_array();
for (x, amm) in out.iter_mut().zip(amount.as_array().iter().copied()) {
    *x = if amm >= 64  {
        0
    } else {
        *x >> amm
    };
}
U64x4::from(out)

Avx2

_mm256_srlv_epi64
- VPSRLVQ ymm, ymm, ymm

type Output = U64x4

The resulting type after applying the >> operator.

source

impl Shr<u64> for U64x4

source

fn shr(self, amount: u64) -> U64x4

Scalar Equivalent:

if amount >= 64 {
    U64x4::ZERO
} else {
    U64x4::from([
        self.as_array()[0] >> amount,
        self.as_array()[1] >> amount,
        self.as_array()[2] >> amount,
        self.as_array()[3] >> amount,
    ])
}

Avx2

_mm256_srl_epi64
- VPSRLQ ymm, ymm, xmm
_mm_set_epi64x

Instruction sequence.

type Output = U64x4

The resulting type after applying the >> operator.

source

impl ShrAssign<U64x4> for U64x4

source

fn shr_assign(&mut self, amount: U64x4)

Performs the >>= operation. Read more

source

impl ShrAssign<u64> for U64x4

source

fn shr_assign(&mut self, amount: u64)

Performs the >>= operation. Read more

source

impl SimdBase for U64x4

source

fn is_zero(&self) -> bool

Scalar Equivalent:

self.as_array().iter().all(|x| *x == 0)

Avx2

_mm256_testz_si256
- VPTEST ymm, ymm

source

fn set_lo(scalar: u64) -> U64x4

Scalar Equivalent:

let mut out = [0; 4];
out[0] = scalar;
U64x4::from(out)

Avx2

_mm256_set_epi64x

Instruction sequence.

source

fn extract<const I: usize>(&self) -> u64

Scalar Equivalent:

self.as_array()[I]

Avx2

_mm256_extract_epi64

Instruction sequence.

source

fn broadcast(scalar: u64) -> U64x4

Scalar Equivalent:

U64x4::from([scalar; 4])

Avx2

_mm256_set1_epi64x

Instruction sequence.

source

fn broadcast_lo(vector: U64x2) -> U64x4

Scalar Equivalent:

U64x4::from([vector.as_array()[0]; 4])

Avx2

_mm256_broadcastq_epi64
- VPBROADCASTQ ymm, xmm

source

fn cmp_eq(&self, other: U64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    if self.as_array()[0] == other.as_array()[0] {  u64::MAX  } else { 0 },
    if self.as_array()[1] == other.as_array()[1] {  u64::MAX  } else { 0 },
    if self.as_array()[2] == other.as_array()[2] {  u64::MAX  } else { 0 },
    if self.as_array()[3] == other.as_array()[3] {  u64::MAX  } else { 0 },
])

Avx2

_mm256_cmpeq_epi64
- VPCMPEQQ ymm, ymm, ymm

source

fn and_not(&self, other: U64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    self.as_array()[0] & (!other.as_array()[0]),
    self.as_array()[1] & (!other.as_array()[1]),
    self.as_array()[2] & (!other.as_array()[2]),
    self.as_array()[3] & (!other.as_array()[3]),
])

Avx2

_mm256_andnot_si256
- VPANDN ymm, ymm, ymm

source

fn cmp_gt(&self, other: U64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    if self.as_array()[0] > other.as_array()[0] {  u64::MAX  } else { 0 },
    if self.as_array()[1] > other.as_array()[1] {  u64::MAX  } else { 0 },
    if self.as_array()[2] > other.as_array()[2] {  u64::MAX  } else { 0 },
    if self.as_array()[3] > other.as_array()[3] {  u64::MAX  } else { 0 },
])

Avx2

NOTE: this implementation uses an efficient vector polyfill, though this operation is not natively supported.

// Based on https://stackoverflow.com/a/33173643 and https://git.io/JmghK
let sign_bit = Self::broadcast(1 << 63);
Self::from(I64x4::from(*self ^ sign_bit).cmp_gt(
    I64x4::from(other ^ sign_bit)
))

source

fn shift_left<const BITS: usize>(&self) -> U64x4

Scalar Equivalent:

let mut out = self.as_array();
for x in out.iter_mut() {
    *x <<= BITS;
}
U64x4::from(out)

Avx2

_mm256_slli_epi64
- VPSLLQ ymm, ymm, imm8

source

fn shift_right<const BITS: usize>(&self) -> U64x4

Scalar Equivalent:

let mut out = self.as_array();
for x in out.iter_mut() {
    *x >>= BITS;
}
U64x4::from(out)

Avx2

_mm256_srli_epi64
- VPSRLQ ymm, ymm, imm8

source

fn unpack_lo(&self, other: U64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    // Lane# 0
    self.as_array()[0],
    other.as_array()[0],
    // Lane# 1
    self.as_array()[2],
    other.as_array()[2],
])

Avx2

_mm256_unpacklo_epi64
- VPUNPCKLQDQ ymm, ymm, ymm

source

fn unpack_hi(&self, other: U64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    // Lane# 0
    self.as_array()[1],
    other.as_array()[1],
    // Lane# 1
    self.as_array()[3],
    other.as_array()[3],
])

Avx2

_mm256_unpackhi_epi64
- VPUNPCKHQDQ ymm, ymm, ymm

source

fn max(&self, other: U64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    self.as_array()[0].max(other.as_array()[0]),
    self.as_array()[1].max(other.as_array()[1]),
    self.as_array()[2].max(other.as_array()[2]),
    self.as_array()[3].max(other.as_array()[3]),
])

Avx2

WARNING: this implementation is a polyfill which executes the scalar implemenation.

source

fn min(&self, other: U64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    self.as_array()[0].min(other.as_array()[0]),
    self.as_array()[1].min(other.as_array()[1]),
    self.as_array()[2].min(other.as_array()[2]),
    self.as_array()[3].min(other.as_array()[3]),
])

Avx2

WARNING: this implementation is a polyfill which executes the scalar implemenation.

type Scalar = u64

The scalar that this value holds.

type Array = [u64 ; 4]

The equivalent array type of this vector.

type Signed = I64x4

The signed version of this vector.

type Unsigned = U64x4

The unsigned version of this vector.

source

const LANES: usize = 4usize

The number of elements of this vector. Read more

source

const ZERO: Self = _

type BroadcastLoInput = U64x2

source

fn as_array(&self) -> Self::Array

Convert the vector to an array.

source

impl SimdBase4x for U64x4

source

fn blend<const B3: bool, const B2: bool, const B1: bool, const B0: bool>(
&self,
if_true: U64x4
) -> U64x4

Scalar Equivalent:

U64x4::from([
        (if B0 { if_true } else { *self }).as_array()[0],
        (if B1 { if_true } else { *self }).as_array()[1],
        (if B2 { if_true } else { *self }).as_array()[2],
        (if B3 { if_true } else { *self }).as_array()[3],
])

Avx2

_mm256_blend_epi32
- VPBLENDD ymm, ymm, ymm, imm8

source

impl SimdBase4x64 for U64x4

source

fn shuffle<const I3: usize, const I2: usize, const I1: usize, const I0: usize>(
&self
) -> U64x4

Scalar Equivalent:

U64x4::from([
    self.as_array()[I0],
    self.as_array()[I1],
    self.as_array()[I2],
    self.as_array()[I3],
])

Avx2

_mm256_permute4x64_epi64
- VPERMQ ymm, ymm, imm8

source

impl SimdBase64 for U64x4

source

fn mul_lo(&self, other: U64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    ((self.as_array()[0] as u32) as u64) * ((other.as_array()[0] as u32) as u64),
    ((self.as_array()[1] as u32) as u64) * ((other.as_array()[1] as u32) as u64),
    ((self.as_array()[2] as u32) as u64) * ((other.as_array()[2] as u32) as u64),
    ((self.as_array()[3] as u32) as u64) * ((other.as_array()[3] as u32) as u64),
])

Avx2

_mm256_mul_epu32
- VPMULUDQ ymm, ymm, ymm

source

impl SimdBaseGatherable<I32x4> for U64x4

Safety

base does not need to be aligned. Forall i, base + indices[i] must meet the safety requirements of std::ptr::read_unaligned

source

unsafe fn gather(base: *const u64, indices: I32x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    base.offset(indices.as_array()[0] as isize).read_unaligned(),
    base.offset(indices.as_array()[1] as isize).read_unaligned(),
    base.offset(indices.as_array()[2] as isize).read_unaligned(),
    base.offset(indices.as_array()[3] as isize).read_unaligned(),
])

Avx2

_mm256_i32gather_epi64
- VPGATHERDQ ymm, vm32x, ymm

source

unsafe fn gather_masked(
    base: *const u64,
    indices: I32x4,
    mask: U64x4,
    src: U64x4
) -> U64x4

Scalar Equivalent:

U64x4::from([
    if (mask.as_array()[0] >> 63) == 1 {
        base.offset(indices.as_array()[0] as isize).read_unaligned()
    } else {
        src.as_array()[0]
    },
    if (mask.as_array()[1] >> 63) == 1 {
        base.offset(indices.as_array()[1] as isize).read_unaligned()
    } else {
        src.as_array()[1]
    },
    if (mask.as_array()[2] >> 63) == 1 {
        base.offset(indices.as_array()[2] as isize).read_unaligned()
    } else {
        src.as_array()[2]
    },
    if (mask.as_array()[3] >> 63) == 1 {
        base.offset(indices.as_array()[3] as isize).read_unaligned()
    } else {
        src.as_array()[3]
    },
])

Avx2

_mm256_mask_i32gather_epi64
- VPGATHERDQ ymm, vm32x, ymm

source

impl SimdBaseGatherable<I64x4> for U64x4

Safety

base does not need to be aligned. Forall i, base + indices[i] must meet the safety requirements of std::ptr::read_unaligned

source

unsafe fn gather(base: *const u64, indices: I64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    base.offset(indices.as_array()[0] as isize).read_unaligned(),
    base.offset(indices.as_array()[1] as isize).read_unaligned(),
    base.offset(indices.as_array()[2] as isize).read_unaligned(),
    base.offset(indices.as_array()[3] as isize).read_unaligned(),
])

Avx2

_mm256_i64gather_epi64
- VPGATHERQQ ymm, vm64x, ymm

source

unsafe fn gather_masked(
    base: *const u64,
    indices: I64x4,
    mask: U64x4,
    src: U64x4
) -> U64x4

Scalar Equivalent:

U64x4::from([
    if (mask.as_array()[0] >> 63) == 1 {
        base.offset(indices.as_array()[0] as isize).read_unaligned()
    } else {
        src.as_array()[0]
    },
    if (mask.as_array()[1] >> 63) == 1 {
        base.offset(indices.as_array()[1] as isize).read_unaligned()
    } else {
        src.as_array()[1]
    },
    if (mask.as_array()[2] >> 63) == 1 {
        base.offset(indices.as_array()[2] as isize).read_unaligned()
    } else {
        src.as_array()[2]
    },
    if (mask.as_array()[3] >> 63) == 1 {
        base.offset(indices.as_array()[3] as isize).read_unaligned()
    } else {
        src.as_array()[3]
    },
])

Avx2

_mm256_mask_i64gather_epi64
- VPGATHERQQ ymm, vm64x, ymm

source

impl SimdBaseGatherable<U64x4> for I32x4

Safety

base does not need to be aligned. Forall i, base + indices[i] must meet the safety requirements of std::ptr::read_unaligned

source

unsafe fn gather(base: *const i32, indices: U64x4) -> I32x4

Scalar Equivalent:

I32x4::from([
    base.offset(indices.as_array()[0] as isize).read_unaligned(),
    base.offset(indices.as_array()[1] as isize).read_unaligned(),
    base.offset(indices.as_array()[2] as isize).read_unaligned(),
    base.offset(indices.as_array()[3] as isize).read_unaligned(),
])

Avx2

_mm256_i64gather_epi32
- VPGATHERQD xmm, vm64y, xmm

source

unsafe fn gather_masked(
    base: *const i32,
    indices: U64x4,
    mask: I32x4,
    src: I32x4
) -> I32x4

Scalar Equivalent:

I32x4::from([
    if ((mask.as_array()[0] as u32) >> 31) == 1 {
        base.offset(indices.as_array()[0] as isize).read_unaligned()
    } else {
        src.as_array()[0]
    },
    if ((mask.as_array()[1] as u32) >> 31) == 1 {
        base.offset(indices.as_array()[1] as isize).read_unaligned()
    } else {
        src.as_array()[1]
    },
    if ((mask.as_array()[2] as u32) >> 31) == 1 {
        base.offset(indices.as_array()[2] as isize).read_unaligned()
    } else {
        src.as_array()[2]
    },
    if ((mask.as_array()[3] as u32) >> 31) == 1 {
        base.offset(indices.as_array()[3] as isize).read_unaligned()
    } else {
        src.as_array()[3]
    },
])

Avx2

_mm256_mask_i64gather_epi32
- VPGATHERQD xmm, vm64y, xmm

source

impl SimdBaseGatherable<U64x4> for I64x4

Safety

base does not need to be aligned. Forall i, base + indices[i] must meet the safety requirements of std::ptr::read_unaligned

source

unsafe fn gather(base: *const i64, indices: U64x4) -> I64x4

Scalar Equivalent:

I64x4::from([
    base.offset(indices.as_array()[0] as isize).read_unaligned(),
    base.offset(indices.as_array()[1] as isize).read_unaligned(),
    base.offset(indices.as_array()[2] as isize).read_unaligned(),
    base.offset(indices.as_array()[3] as isize).read_unaligned(),
])

Avx2

_mm256_i64gather_epi64
- VPGATHERQQ ymm, vm64x, ymm

source

unsafe fn gather_masked(
    base: *const i64,
    indices: U64x4,
    mask: I64x4,
    src: I64x4
) -> I64x4

Scalar Equivalent:

I64x4::from([
    if ((mask.as_array()[0] as u64) >> 63) == 1 {
        base.offset(indices.as_array()[0] as isize).read_unaligned()
    } else {
        src.as_array()[0]
    },
    if ((mask.as_array()[1] as u64) >> 63) == 1 {
        base.offset(indices.as_array()[1] as isize).read_unaligned()
    } else {
        src.as_array()[1]
    },
    if ((mask.as_array()[2] as u64) >> 63) == 1 {
        base.offset(indices.as_array()[2] as isize).read_unaligned()
    } else {
        src.as_array()[2]
    },
    if ((mask.as_array()[3] as u64) >> 63) == 1 {
        base.offset(indices.as_array()[3] as isize).read_unaligned()
    } else {
        src.as_array()[3]
    },
])

Avx2

_mm256_mask_i64gather_epi64
- VPGATHERQQ ymm, vm64x, ymm

source

impl SimdBaseGatherable<U64x4> for U32x4

Safety

base does not need to be aligned. Forall i, base + indices[i] must meet the safety requirements of std::ptr::read_unaligned

source

unsafe fn gather(base: *const u32, indices: U64x4) -> U32x4

Scalar Equivalent:

U32x4::from([
    base.offset(indices.as_array()[0] as isize).read_unaligned(),
    base.offset(indices.as_array()[1] as isize).read_unaligned(),
    base.offset(indices.as_array()[2] as isize).read_unaligned(),
    base.offset(indices.as_array()[3] as isize).read_unaligned(),
])

Avx2

_mm256_i64gather_epi32
- VPGATHERQD xmm, vm64y, xmm

source

unsafe fn gather_masked(
    base: *const u32,
    indices: U64x4,
    mask: U32x4,
    src: U32x4
) -> U32x4

Scalar Equivalent:

U32x4::from([
    if (mask.as_array()[0] >> 31) == 1 {
        base.offset(indices.as_array()[0] as isize).read_unaligned()
    } else {
        src.as_array()[0]
    },
    if (mask.as_array()[1] >> 31) == 1 {
        base.offset(indices.as_array()[1] as isize).read_unaligned()
    } else {
        src.as_array()[1]
    },
    if (mask.as_array()[2] >> 31) == 1 {
        base.offset(indices.as_array()[2] as isize).read_unaligned()
    } else {
        src.as_array()[2]
    },
    if (mask.as_array()[3] >> 31) == 1 {
        base.offset(indices.as_array()[3] as isize).read_unaligned()
    } else {
        src.as_array()[3]
    },
])

Avx2

_mm256_mask_i64gather_epi32
- VPGATHERQD xmm, vm64y, xmm

source

impl SimdBaseGatherable<U64x4> for U64x4

Safety

base does not need to be aligned. Forall i, base + indices[i] must meet the safety requirements of std::ptr::read_unaligned

source

unsafe fn gather(base: *const u64, indices: U64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    base.offset(indices.as_array()[0] as isize).read_unaligned(),
    base.offset(indices.as_array()[1] as isize).read_unaligned(),
    base.offset(indices.as_array()[2] as isize).read_unaligned(),
    base.offset(indices.as_array()[3] as isize).read_unaligned(),
])

Avx2

_mm256_i64gather_epi64
- VPGATHERQQ ymm, vm64x, ymm

source

unsafe fn gather_masked(
    base: *const u64,
    indices: U64x4,
    mask: U64x4,
    src: U64x4
) -> U64x4

Scalar Equivalent:

U64x4::from([
    if (mask.as_array()[0] >> 63) == 1 {
        base.offset(indices.as_array()[0] as isize).read_unaligned()
    } else {
        src.as_array()[0]
    },
    if (mask.as_array()[1] >> 63) == 1 {
        base.offset(indices.as_array()[1] as isize).read_unaligned()
    } else {
        src.as_array()[1]
    },
    if (mask.as_array()[2] >> 63) == 1 {
        base.offset(indices.as_array()[2] as isize).read_unaligned()
    } else {
        src.as_array()[2]
    },
    if (mask.as_array()[3] >> 63) == 1 {
        base.offset(indices.as_array()[3] as isize).read_unaligned()
    } else {
        src.as_array()[3]
    },
])

Avx2

_mm256_mask_i64gather_epi64
- VPGATHERQQ ymm, vm64x, ymm

source

impl Sub<U64x4> for U64x4

source

fn sub(self, rhs: U64x4) -> U64x4

Scalar Equivalent:

U64x4::from([
    self.as_array()[0].wrapping_sub(rhs.as_array()[0]),
    self.as_array()[1].wrapping_sub(rhs.as_array()[1]),
    self.as_array()[2].wrapping_sub(rhs.as_array()[2]),
    self.as_array()[3].wrapping_sub(rhs.as_array()[3]),
])

Avx2

_mm256_sub_epi64
- VPSUBQ ymm, ymm, ymm

type Output = U64x4

The resulting type after applying the - operator.

source

impl SubAssign<U64x4> for U64x4

source

fn sub_assign(&mut self, rhs: Self)

Performs the -= operation. Read more

source

impl Zeroable for U64x4

impl Pod for U64x4

Auto Trait Implementations

impl RefUnwindSafe for U64x4

impl Send for U64x4

impl Sync for U64x4

impl Unpin for U64x4

impl UnwindSafe for U64x4

Blanket Implementations

source

impl<T> Any for Twhere
T: 'static + ?Sized,

source

fn type_id(&self) -> TypeId

Gets the TypeId of self. Read more

source

impl<T> Borrow<T> for Twhere
T: ?Sized,

const: unstable · source

fn borrow(&self) -> &T

Immutably borrows from an owned value. Read more

source

impl<T> BorrowMut<T> for Twhere
T: ?Sized,

const: unstable · source

fn borrow_mut(&mut self) -> &mut T

Mutably borrows from an owned value. Read more

impl<T> CheckedBitPattern for Twhere
T: AnyBitPattern,

type Bits = T

Self must have the same layout as the specified Bits except for the possible invalid bit patterns being checked during is_valid_bit_pattern. Read more

fn is_valid_bit_pattern(_bits: &T) -> bool

If this function returns true, then it must be valid to reinterpret bits as &Self. Read more

source

impl<T> From<T> for T

const: unstable · source

fn from(t: T) -> T

Returns the argument unchanged.

source

impl<T, U> Into for Twhere
U: From<T>,

const: unstable · source

fn into(self) -> U

Calls U::from(self).

That is, this conversion is whatever the implementation of From<T> for U chooses to do.

source

impl<T> Same<T> for T

type Output = T

Should always be Self

source

impl<T> ToOwned for Twhere
T: Clone,

type Owned = T

The resulting type after obtaining ownership.

source

fn to_owned(&self) -> T

Creates owned data from borrowed data, usually by cloning. Read more

source

fn clone_into(&self, target: &mut T)

Uses borrowed data to replace owned data, usually by cloning. Read more

source

impl<T, U> TryFrom for Twhere
U: Into<T>,

type Error = Infallible

The type returned in the event of a conversion error.

const: unstable · source

fn try_from(value: U) -> Result<T, <T as TryFrom>::Error>

Performs the conversion.

source

impl<T, U> TryInto for Twhere
U: TryFrom<T>,

type Error = >::Error

The type returned in the event of a conversion error.

const: unstable · source

fn try_into(self) -> Result<U, >::Error>

Performs the conversion.

Struct vectoreyes::U64x4

Implementations

impl U64x4

pub const fn from_array(array: [u64; 4]) -> U64x4

Trait Implementations

impl Add<U64x4> for U64x4

fn add(self, rhs: U64x4) -> U64x4

type Output = U64x4

impl AddAssign<U64x4> for U64x4

fn add_assign(&mut self, rhs: Self)

impl BitAnd<U64x4> for U64x4

fn bitand(self, rhs: U64x4) -> U64x4

type Output = U64x4

impl BitAndAssign<U64x4> for U64x4

fn bitand_assign(&mut self, rhs: Self)

impl BitOr<U64x4> for U64x4

fn bitor(self, rhs: U64x4) -> U64x4

type Output = U64x4

impl BitOrAssign<U64x4> for U64x4

fn bitor_assign(&mut self, rhs: Self)

impl BitXor<U64x4> for U64x4

fn bitxor(self, rhs: U64x4) -> U64x4

type Output = U64x4

impl BitXorAssign<U64x4> for U64x4

fn bitxor_assign(&mut self, rhs: Self)

impl Clone for U64x4

fn clone(&self) -> U64x4

fn clone_from(&mut self, source: &Self)

impl ConditionallySelectable for U64x4

fn conditional_select(a: &Self, b: &Self, choice: Choice) -> Self

fn conditional_assign(&mut self, other: &Self, choice: Choice)

fn conditional_swap(a: &mut Self, b: &mut Self, choice: Choice)

impl ConstantTimeEq for U64x4

fn ct_eq(&self, other: &Self) -> Choice

impl Debug for U64x4

fn fmt(&self, f: &mut Formatter<'_>) -> Result

impl Default for U64x4

fn default() -> Self

impl ExtendingCast<U16x8> for U64x4

fn extending_cast_from(vector: U16x8) -> U64x4

impl ExtendingCast<U32x4> for U64x4

fn extending_cast_from(vector: U32x4) -> U64x4

impl ExtendingCast<U8x16> for U64x4

fn extending_cast_from(vector: U8x16) -> U64x4

impl From<[U64x2; 2]> for U64x4

fn from(vectors: [U64x2; 2]) -> U64x4

impl From<[u64; 4]> for U64x4

fn from(array: [u64; 4]) -> U64x4

impl From<I16x16> for U64x4

fn from(x: I16x16) -> U64x4

impl From<I32x8> for U64x4

fn from(x: I32x8) -> U64x4

impl From<I64x4> for U64x4

fn from(x: I64x4) -> U64x4

impl From<I8x32> for U64x4

fn from(x: I8x32) -> U64x4

impl From<U16x16> for U64x4

fn from(x: U16x16) -> U64x4

impl From<U32x4> for U64x4

fn from(vector: U32x4) -> U64x4

impl From<U32x8> for U64x4

fn from(x: U32x8) -> U64x4

impl From<U64x2> for U64x4

fn from(vector: U64x2) -> U64x4

impl From<U64x4> for [U64x2; 2]

fn from(vector: U64x4) -> [U64x2; 2]

impl From<U64x4> for [u64; 4]

fn from(vector: U64x4) -> [u64; 4]

impl From<U64x4> for I16x16

fn from(x: U64x4) -> I16x16

impl From<U64x4> for I32x8

fn from(x: U64x4) -> I32x8

impl From<U64x4> for I64x4

fn from(x: U64x4) -> I64x4

impl From<U64x4> for I8x32

fn from(x: U64x4) -> I8x32

impl From<U64x4> for U16x16

fn from(x: U64x4) -> U16x16

impl From<U64x4> for U32x8

fn from(x: U64x4) -> U32x8

pub const fn from_array(array: [u64 ; 4]) -> U64x4

impl From<[U64x2 ; 2]> for U64x4

fn from(vectors: [U64x2 ; 2]) -> U64x4

impl From<[u64 ; 4]> for U64x4

fn from(array: [u64 ; 4]) -> U64x4

impl From<U64x4> for [U64x2 ; 2]

fn from(vector: U64x4) -> [U64x2 ; 2]

impl From<U64x4> for [u64 ; 4]

fn from(vector: U64x4) -> [u64 ; 4]

fn hash_slice<H>(data: &[Self], state: &mut H)where
H: Hasher,