Struct vectoreyes::I32x4

source · [−]

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

Expand description

[i32; 4] as a vector.

Implementations

source

impl I32x4

source

pub const fn from_array(array: [i32 ; 4]) -> I32x4

Create a vector from an array.

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

Example

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

Avx2

Trait Implementations

source

impl Add<I32x4> for I32x4

source

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

Scalar Equivalent:

I32x4::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

_mm_add_epi32
- PADDD xmm, xmm

type Output = I32x4

The resulting type after applying the + operator.

source

impl AddAssign<I32x4> for I32x4

source

fn add_assign(&mut self, rhs: Self)

Performs the += operation. Read more

source

impl BitAnd<I32x4> for I32x4

source

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

Scalar Equivalent:

I32x4::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

_mm_and_si128
- PAND xmm, xmm

type Output = I32x4

The resulting type after applying the & operator.

source

impl BitAndAssign<I32x4> for I32x4

source

fn bitand_assign(&mut self, rhs: Self)

Performs the &= operation. Read more

source

impl BitOr<I32x4> for I32x4

source

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

Scalar Equivalent:

I32x4::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

_mm_or_si128
- POR xmm, xmm

type Output = I32x4

The resulting type after applying the | operator.

source

impl BitOrAssign<I32x4> for I32x4

source

fn bitor_assign(&mut self, rhs: Self)

Performs the |= operation. Read more

source

impl BitXor<I32x4> for I32x4

source

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

Scalar Equivalent:

I32x4::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

_mm_xor_si128
- PXOR xmm, xmm

type Output = I32x4

The resulting type after applying the ^ operator.

source

impl BitXorAssign<I32x4> for I32x4

source

fn bitxor_assign(&mut self, rhs: Self)

Performs the ^= operation. Read more

source

impl Clone for I32x4

source

fn clone(&self) -> I32x4

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 I32x4

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 I32x4

source

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

Determine if two items are equal. Read more

source

impl Debug for I32x4

source

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

Formats the value using the given formatter. Read more

source

impl Default for I32x4

source

fn default() -> Self

The zero vector.

source

impl ExtendingCast<I16x8> for I32x4

source

fn extending_cast_from(vector: I16x8) -> I32x4

Scalar Equivalent:

I32x4::from([
        i32::from(vector.as_array()[0]),
        i32::from(vector.as_array()[1]),
        i32::from(vector.as_array()[2]),
        i32::from(vector.as_array()[3]),
])

Avx2

_mm_cvtepi16_epi32
- PMOVSXWD xmm, xmm

source

impl ExtendingCast<I32x4> for I64x2

source

fn extending_cast_from(vector: I32x4) -> I64x2

Scalar Equivalent:

I64x2::from([
        i64::from(vector.as_array()[0]),
        i64::from(vector.as_array()[1]),
])

Avx2

_mm_cvtepi32_epi64
- PMOVSXDQ xmm, xmm

source

impl ExtendingCast<I32x4> for I64x4

source

fn extending_cast_from(vector: I32x4) -> I64x4

Scalar Equivalent:

I64x4::from([
        i64::from(vector.as_array()[0]),
        i64::from(vector.as_array()[1]),
        i64::from(vector.as_array()[2]),
        i64::from(vector.as_array()[3]),
])

Avx2

_mm256_cvtepi32_epi64
- VPMOVSXDQ ymm, xmm

source

impl ExtendingCast<I8x16> for I32x4

source

fn extending_cast_from(vector: I8x16) -> I32x4

Scalar Equivalent:

I32x4::from([
        i32::from(vector.as_array()[0]),
        i32::from(vector.as_array()[1]),
        i32::from(vector.as_array()[2]),
        i32::from(vector.as_array()[3]),
])

Avx2

_mm_cvtepi8_epi32
- PMOVSXBD xmm, xmm

source

impl From<[i32 ; 4]> for I32x4

source

fn from(array: [i32 ; 4]) -> I32x4

Avx2

_mm_loadu_si128
- MOVDQU xmm, m128

source

impl From<I16x8> for I32x4

source

fn from(x: I16x8) -> I32x4

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

source

impl From<I32x4> for [i32 ; 4]

source

fn from(vector: I32x4) -> [i32 ; 4]

Avx2

_mm_storeu_si128
- MOVDQU m128, xmm

source

impl From<I32x4> for I16x8

source

fn from(x: I32x4) -> I16x8

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

source

impl From<I32x4> for I32x8

source

fn from(vector: I32x4) -> I32x8

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; 8];
out[0..4].copy_from_slice(&vector.as_array());
I32x8::from(out)

Avx2

_mm256_zextsi128_si256

source

impl From<I32x4> for I64x2

source

fn from(x: I32x4) -> I64x2

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

source

impl From<I32x4> for I64x4

source

fn from(vector: I32x4) -> I64x4

Scalar Equivalent:

I64x4::from([
        i64::from(vector.as_array()[0]),
        i64::from(vector.as_array()[1]),
        i64::from(vector.as_array()[2]),
        i64::from(vector.as_array()[3]),
])

Avx2

_mm256_cvtepi32_epi64
- VPMOVSXDQ ymm, xmm

source

impl From<I32x4> for I8x16

source

fn from(x: I32x4) -> I8x16

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

source

impl From<I32x4> for U16x8

source

fn from(x: I32x4) -> U16x8

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

source

impl From<I32x4> for U32x4

source

fn from(x: I32x4) -> U32x4

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

source

impl From<I32x4> for U64x2

source

fn from(x: I32x4) -> U64x2

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

source

impl From<I32x4> for U8x16

source

fn from(x: I32x4) -> U8x16

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

source

impl From<I64x2> for I32x4

source

fn from(x: I64x2) -> I32x4

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

source

impl From<I8x16> for I32x4

source

fn from(x: I8x16) -> I32x4

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

source

impl From<U16x8> for I32x4

source

fn from(x: U16x8) -> I32x4

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

source

impl From<U32x4> for I32x4

source

fn from(x: U32x4) -> I32x4

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

source

impl From<U64x2> for I32x4

source

fn from(x: U64x2) -> I32x4

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

source

impl From<U8x16> for I32x4

source

fn from(x: U8x16) -> I32x4

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

source

impl Hash for I32x4

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<I32x4> for I32x4

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<I32x4> for I32x4

source

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

Scalar Equivalent:

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

Avx2

_mm_sllv_epi32
- VPSLLVD xmm, xmm, xmm

type Output = I32x4

The resulting type after applying the << operator.

source

impl Shl<u64> for I32x4

source

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

Scalar Equivalent:

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

Avx2

_mm_set_epi64x

Instruction sequence.
_mm_sll_epi32
- PSLLD xmm, xmm

type Output = I32x4

The resulting type after applying the << operator.

source

impl ShlAssign<I32x4> for I32x4

source

fn shl_assign(&mut self, amount: I32x4)

Performs the <<= operation. Read more

source

impl ShlAssign<u64> for I32x4

source

fn shl_assign(&mut self, amount: u64)

Performs the <<= operation. Read more

source

impl Shr<I32x4> for I32x4

source

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

Scalar Equivalent:

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

Avx2

_mm_srav_epi32
- VPSRAVD xmm, xmm, xmm

type Output = I32x4

The resulting type after applying the >> operator.

source

impl Shr<u64> for I32x4

source

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

Scalar Equivalent:

if amount >= 32 {
    let mut out = self.as_array();
    for x in out.iter_mut() {
        *x = if *x < 0 { -1 } else { 0 };
    }
    I32x4::from(out)
} else {
    I32x4::from([
        self.as_array()[0] >> amount,
        self.as_array()[1] >> amount,
        self.as_array()[2] >> amount,
        self.as_array()[3] >> amount,
    ])
}

Avx2

_mm_set_epi64x

Instruction sequence.
_mm_sra_epi32
- PSRAD xmm, xmm

type Output = I32x4

The resulting type after applying the >> operator.

source

impl ShrAssign<I32x4> for I32x4

source

fn shr_assign(&mut self, amount: I32x4)

Performs the >>= operation. Read more

source

impl ShrAssign<u64> for I32x4

source

fn shr_assign(&mut self, amount: u64)

Performs the >>= operation. Read more

source

impl SimdBase for I32x4

source

fn is_zero(&self) -> bool

Scalar Equivalent:

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

Avx2

_mm_testz_si128
- PTEST xmm, xmm

source

fn set_lo(scalar: i32) -> I32x4

Scalar Equivalent:

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

Avx2

_mm_set_epi32

Instruction sequence.

source

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

Scalar Equivalent:

self.as_array()[I]

Avx2

_mm_extract_epi32
- PEXTRD r32, xmm, imm8

source

fn broadcast(scalar: i32) -> I32x4

Scalar Equivalent:

I32x4::from([scalar; 4])

Avx2

_mm_set1_epi32

Instruction sequence.

source

fn broadcast_lo(vector: I32x4) -> I32x4

Scalar Equivalent:

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

Avx2

_mm_broadcastd_epi32
- VPBROADCASTD xmm, xmm

source

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

Scalar Equivalent:

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

Avx2

_mm_cmpeq_epi32
- PCMPEQD xmm, xmm

source

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

Scalar Equivalent:

I32x4::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

_mm_andnot_si128
- PANDN xmm, xmm

source

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

Scalar Equivalent:

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

Avx2

_mm_cmpgt_epi32
- PCMPGTD xmm, xmm

source

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

Scalar Equivalent:

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

Avx2

_mm_slli_epi32
- PSLLD xmm, imm8

source

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

Scalar Equivalent:

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

Avx2

_mm_srai_epi32
- PSRAD xmm, imm8

source

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

Scalar Equivalent:

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

Avx2

_mm_unpacklo_epi32
- PUNPCKLDQ xmm, xmm

source

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

Scalar Equivalent:

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

Avx2

_mm_unpackhi_epi32
- PUNPCKHDQ xmm, xmm

source

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

Scalar Equivalent:

I32x4::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

_mm_max_epi32
- PMAXSD xmm, xmm

source

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

Scalar Equivalent:

I32x4::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

_mm_min_epi32
- PMINSD xmm, xmm

type Scalar = i32

The scalar that this value holds.

type Array = [i32 ; 4]

The equivalent array type of this vector.

type Signed = I32x4

The signed version of this vector.

type Unsigned = U32x4

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 = I32x4

source

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

Convert the vector to an array.

source

impl SimdBase32 for I32x4

source

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

Scalar Equivalent:

I32x4::from([
    // 128-bit Lane #0
    self.as_array()[I0 + 0 * 4],
    self.as_array()[I1 + 0 * 4],
    self.as_array()[I2 + 0 * 4],
    self.as_array()[I3 + 0 * 4],
])

Avx2

_mm_shuffle_epi32
- PSHUFD xmm, xmm, imm8

source

impl SimdBase4x for I32x4

source

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

Scalar Equivalent:

I32x4::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

_mm_blend_epi32
- VPBLENDD xmm, xmm, xmm, imm8

source

impl SimdBaseGatherable<I32x4> 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: I32x4) -> 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

_mm_i32gather_epi32
- VPGATHERDD xmm, vm32x, xmm

source

unsafe fn gather_masked(
    base: *const i32,
    indices: I32x4,
    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

_mm_mask_i32gather_epi32
- VPGATHERDD xmm, vm32x, xmm

source

impl SimdBaseGatherable<I32x4> 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: I32x4) -> 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_i32gather_epi64
- VPGATHERDQ ymm, vm32x, ymm

source

unsafe fn gather_masked(
    base: *const i64,
    indices: I32x4,
    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_i32gather_epi64
- VPGATHERDQ ymm, vm32x, ymm

source

impl SimdBaseGatherable<I32x4> 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: I32x4) -> 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

_mm_i32gather_epi32
- VPGATHERDD xmm, vm32x, xmm

source

unsafe fn gather_masked(
    base: *const u32,
    indices: I32x4,
    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

_mm_mask_i32gather_epi32
- VPGATHERDD xmm, vm32x, xmm

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 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: I64x4) -> 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: I64x4,
    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 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 Sub<I32x4> for I32x4

source

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

Scalar Equivalent:

I32x4::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

_mm_sub_epi32
- PSUBD xmm, xmm

type Output = I32x4

The resulting type after applying the - operator.

source

impl SubAssign<I32x4> for I32x4

source

fn sub_assign(&mut self, rhs: Self)

Performs the -= operation. Read more

source

impl Zeroable for I32x4

impl Pod for I32x4

Auto Trait Implementations

impl RefUnwindSafe for I32x4

impl Send for I32x4

impl Sync for I32x4

impl Unpin for I32x4

impl UnwindSafe for I32x4

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::I32x4

Implementations

impl I32x4

pub const fn from_array(array: [i32; 4]) -> I32x4

Trait Implementations

impl Add<I32x4> for I32x4

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

type Output = I32x4

impl AddAssign<I32x4> for I32x4

fn add_assign(&mut self, rhs: Self)

impl BitAnd<I32x4> for I32x4

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

type Output = I32x4

impl BitAndAssign<I32x4> for I32x4

fn bitand_assign(&mut self, rhs: Self)

impl BitOr<I32x4> for I32x4

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

type Output = I32x4

impl BitOrAssign<I32x4> for I32x4

fn bitor_assign(&mut self, rhs: Self)

impl BitXor<I32x4> for I32x4

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

type Output = I32x4

impl BitXorAssign<I32x4> for I32x4

fn bitxor_assign(&mut self, rhs: Self)

impl Clone for I32x4

fn clone(&self) -> I32x4

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

impl ConditionallySelectable for I32x4

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 I32x4

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

impl Debug for I32x4

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

impl Default for I32x4

fn default() -> Self

impl ExtendingCast<I16x8> for I32x4

fn extending_cast_from(vector: I16x8) -> I32x4

impl ExtendingCast<I32x4> for I64x2

fn extending_cast_from(vector: I32x4) -> I64x2

impl ExtendingCast<I32x4> for I64x4

fn extending_cast_from(vector: I32x4) -> I64x4

impl ExtendingCast<I8x16> for I32x4

fn extending_cast_from(vector: I8x16) -> I32x4

impl From<[i32; 4]> for I32x4

fn from(array: [i32; 4]) -> I32x4

impl From<I16x8> for I32x4

fn from(x: I16x8) -> I32x4

impl From<I32x4> for [i32; 4]

fn from(vector: I32x4) -> [i32; 4]

impl From<I32x4> for I16x8

fn from(x: I32x4) -> I16x8

impl From<I32x4> for I32x8

fn from(vector: I32x4) -> I32x8

impl From<I32x4> for I64x2

fn from(x: I32x4) -> I64x2

impl From<I32x4> for I64x4

fn from(vector: I32x4) -> I64x4

impl From<I32x4> for I8x16

fn from(x: I32x4) -> I8x16

impl From<I32x4> for U16x8

fn from(x: I32x4) -> U16x8

impl From<I32x4> for U32x4

fn from(x: I32x4) -> U32x4

impl From<I32x4> for U64x2

fn from(x: I32x4) -> U64x2

impl From<I32x4> for U8x16

fn from(x: I32x4) -> U8x16

impl From<I64x2> for I32x4

fn from(x: I64x2) -> I32x4

impl From<I8x16> for I32x4

fn from(x: I8x16) -> I32x4

impl From<U16x8> for I32x4

fn from(x: U16x8) -> I32x4

impl From<U32x4> for I32x4

fn from(x: U32x4) -> I32x4

impl From<U64x2> for I32x4

fn from(x: U64x2) -> I32x4

pub const fn from_array(array: [i32 ; 4]) -> I32x4

impl From<[i32 ; 4]> for I32x4

fn from(array: [i32 ; 4]) -> I32x4

impl From<I32x4> for [i32 ; 4]

fn from(vector: I32x4) -> [i32 ; 4]

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