Struct U64x2

pub struct U64x2(/* private fields */);

[u64; 2] as a vector.

Implementations

impl U64x2

pub const fn from_array(arr: [u64; 2]) -> Self

Create a vector from an array.

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

Example

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

impl U64x2

pub fn carryless_mul<const HI_OTHER: bool, const HI_SELF: bool>( &self, other: U64x2, ) -> U64x2

Scalar Equivalent:

 let x = if HI_SELF { self.as_array()[1] } else { self.as_array()[0] };
 let y = if HI_OTHER { other.as_array()[1] } else { other.as_array()[0] };
// This software carryless-multplication implementation is from https://github.com/RustCrypto/universal-hashes/blob/2e8a948dbb25bc2ac6c712b4bdc21b158527ca70/polyval/src/backend/soft64.rs
// That code is MIT/Apache dual-licensed.
#[inline(always)]
fn bmul64(x: u64, y: u64) -> u64 {
    use std::num::Wrapping;
    let x0 = Wrapping(x & 0x1111_1111_1111_1111);
    let x1 = Wrapping(x & 0x2222_2222_2222_2222);
    let x2 = Wrapping(x & 0x4444_4444_4444_4444);
    let x3 = Wrapping(x & 0x8888_8888_8888_8888);
    let y0 = Wrapping(y & 0x1111_1111_1111_1111);
    let y1 = Wrapping(y & 0x2222_2222_2222_2222);
    let y2 = Wrapping(y & 0x4444_4444_4444_4444);
    let y3 = Wrapping(y & 0x8888_8888_8888_8888);
    let mut z0 = ((x0 * y0) ^ (x1 * y3) ^ (x2 * y2) ^ (x3 * y1)).0;
    let mut z1 = ((x0 * y1) ^ (x1 * y0) ^ (x2 * y3) ^ (x3 * y2)).0;
    let mut z2 = ((x0 * y2) ^ (x1 * y1) ^ (x2 * y0) ^ (x3 * y3)).0;
    let mut z3 = ((x0 * y3) ^ (x1 * y2) ^ (x2 * y1) ^ (x3 * y0)).0;
    z0 &= 0x1111_1111_1111_1111;
    z1 &= 0x2222_2222_2222_2222;
    z2 &= 0x4444_4444_4444_4444;
    z3 &= 0x8888_8888_8888_8888;
    z0 | z1 | z2 | z3
}
#[inline(always)]
fn rev64(mut x: u64) -> u64 {
    x = ((x & 0x5555_5555_5555_5555) << 1) | ((x >> 1) & 0x5555_5555_5555_5555);
    x = ((x & 0x3333_3333_3333_3333) << 2) | ((x >> 2) & 0x3333_3333_3333_3333);
    x = ((x & 0x0f0f_0f0f_0f0f_0f0f) << 4) | ((x >> 4) & 0x0f0f_0f0f_0f0f_0f0f);
    x = ((x & 0x00ff_00ff_00ff_00ff) << 8) | ((x >> 8) & 0x00ff_00ff_00ff_00ff);
    x = ((x & 0xffff_0000_ffff) << 16) | ((x >> 16) & 0xffff_0000_ffff);
    x.rotate_right(32)
}
U64x2::from([
    bmul64(x, y),
    rev64(bmul64(rev64(x), rev64(y))) >> 1,
])

Avx2

• _mm_clmulepi64_si128

  • PCLMULQDQ xmm, xmm, imm8

Trait Implementations

impl Add for U64x2

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

Perform a pairwise wrapping_add

Scalar Equivalent

U64x2::from([
    self.as_array()[0].wrapping_add(rhs.as_array()[0]),
    self.as_array()[1].wrapping_add(rhs.as_array()[1]),
])

AVX2 Intrinsics Used

• _mm_add_epi64
  • PADDQ xmm, xmm

Neon Intrinsics Used

• vaddq_u64
  • This intrinsic compiles to the following instructions:
    • ADD Vd.2D,Vn.2D,Vm.2D

type Output = U64x2

The resulting type after applying the + operator.

impl AddAssign for U64x2

fn add_assign(&mut self, other: U64x2)

Performs the += operation.

impl AsMut<[u64]> for U64x2

fn as_mut(&mut self) -> &mut [u64]

Converts this type into a mutable reference of the (usually inferred) input type.

impl AsRef<[u64]> for U64x2

fn as_ref(&self) -> &[u64]

Converts this type into a shared reference of the (usually inferred) input type.

impl BitAnd for U64x2

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

Perform a pairwise bitwise and

Scalar Equivalent

U64x2::from([
    self.as_array()[0] & rhs.as_array()[0],
    self.as_array()[1] & rhs.as_array()[1],
])

AVX2 Intrinsics Used

• _mm_and_si128
  • PAND xmm, xmm

Neon Intrinsics Used

• vandq_u64
  • This intrinsic compiles to the following instructions:
    • AND Vd.16B,Vn.16B,Vm.16B

type Output = U64x2

The resulting type after applying the & operator.

impl BitAndAssign for U64x2

fn bitand_assign(&mut self, other: U64x2)

Performs the &= operation.

impl BitOr for U64x2

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

Perform a pairwise bitwise or

Scalar Equivalent

U64x2::from([
    self.as_array()[0] | rhs.as_array()[0],
    self.as_array()[1] | rhs.as_array()[1],
])

AVX2 Intrinsics Used

• _mm_or_si128
  • POR xmm, xmm

Neon Intrinsics Used

• vorrq_u64
  • This intrinsic compiles to the following instructions:
    • ORR Vd.16B,Vn.16B,Vm.16B

type Output = U64x2

The resulting type after applying the | operator.

impl BitOrAssign for U64x2

fn bitor_assign(&mut self, other: U64x2)

Performs the |= operation.

impl BitXor for U64x2

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

Perform a pairwise bitwise xor

Scalar Equivalent

U64x2::from([
    self.as_array()[0] ^ rhs.as_array()[0],
    self.as_array()[1] ^ rhs.as_array()[1],
])

AVX2 Intrinsics Used

• _mm_xor_si128
  • PXOR xmm, xmm

Neon Intrinsics Used

• veorq_u64
  • This intrinsic compiles to the following instructions:
    • EOR Vd.16B,Vn.16B,Vm.16B

type Output = U64x2

The resulting type after applying the ^ operator.

impl BitXorAssign for U64x2

fn bitxor_assign(&mut self, other: U64x2)

Performs the ^= operation.

impl Clone for U64x2

fn clone(&self) -> U64x2

Returns a duplicate of the value.

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

Performs copy-assignment from source.

impl ConditionallySelectable for U64x2

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

Select a or b according to choice.

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

Conditionally assign other to self, according to choice.

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

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

impl ConstantTimeEq for U64x2

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

Determine if two items are equal.

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

Determine if two items are NOT equal.

impl Debug for U64x2

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

Formats the value using the given formatter.

impl Default for U64x2

fn default() -> Self

The zero vector.

impl<'de> Deserialize<'de> for U64x2

fn deserialize<D>(deserializer: D) -> Result<Self, D::Error>

where D: Deserializer<'de>,

Deserialize this value from the given Serde deserializer.

impl Distribution<U64x2> for Standard

fn sample<R: Rng + ?Sized>(&self, rng: &mut R) -> U64x2

Generate a random value of T, using rng as the source of randomness.

fn sample_iter<R>(self, rng: R) -> DistIter<Self, R, T>

where R: Rng, Self: Sized,

Create an iterator that generates random values of T, using rng as the source of randomness.

fn map<F, S>(self, func: F) -> DistMap<Self, F, T, S>

where F: Fn(T) -> S, Self: Sized,

Create a distribution of values of ‘S’ by mapping the output of Self through the closure F

impl ExtendingCast<U16x8> for U64x2

fn extending_cast_from(vector: U16x8) -> U64x2

Scalar Equivalent:

U64x2::from([
        u64::from(vector.as_array()[0]),
        u64::from(vector.as_array()[1]),
])

Avx2

• _mm_cvtepu16_epi64

  • PMOVZXWQ xmm, xmm

impl ExtendingCast<U32x4> for U64x2

fn extending_cast_from(vector: U32x4) -> U64x2

Scalar Equivalent:

U64x2::from([
        u64::from(vector.as_array()[0]),
        u64::from(vector.as_array()[1]),
])

Avx2

• _mm_cvtepu32_epi64

  • PMOVZXDQ xmm, xmm

impl ExtendingCast<U8x16> for U64x2

fn extending_cast_from(vector: U8x16) -> U64x2

Scalar Equivalent:

U64x2::from([
        u64::from(vector.as_array()[0]),
        u64::from(vector.as_array()[1]),
])

Avx2

• _mm_cvtepu8_epi64

  • PMOVZXBQ xmm, xmm

impl From<[u64; 2]> for U64x2

fn from(arr: [u64; 2]) -> U64x2

Converts to this type from the input type.

impl From<I16x8> for U64x2

fn from(x: I16x8) -> U64x2

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

impl From<I32x4> for U64x2

fn from(x: I32x4) -> U64x2

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

impl From<I64x2> for U64x2

fn from(x: I64x2) -> U64x2

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

impl From<I8x16> for U64x2

fn from(x: I8x16) -> U64x2

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

impl From<U16x8> for U64x2

fn from(x: U16x8) -> U64x2

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

impl From<U32x4> for U64x2

fn from(x: U32x4) -> U64x2

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

impl From<U64x2> for [u64; 2]

fn from(arr: U64x2) -> [u64; 2]

Converts to this type from the input type.

impl From<U64x2> for I16x8

fn from(x: U64x2) -> I16x8

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

impl From<U64x2> for I32x4

fn from(x: U64x2) -> I32x4

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

impl From<U64x2> for I64x2

fn from(x: U64x2) -> I64x2

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

impl From<U64x2> for I8x16

fn from(x: U64x2) -> I8x16

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

impl From<U64x2> for U16x8

fn from(x: U64x2) -> U16x8

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

impl From<U64x2> for U32x4

fn from(x: U64x2) -> U32x4

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

impl From<U64x2> for U64x4

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

impl From<U64x2> for U8x16

fn from(x: U64x2) -> U8x16

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

impl From<U8x16> for U64x2

fn from(x: U8x16) -> U64x2

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

impl Hash for U64x2

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

Feeds this value into the given Hasher.

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

where H: Hasher, Self: Sized,

Feeds a slice of this type into the given Hasher.

impl PartialEq for U64x2

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

Tests for self and other values to be equal, and is used by ==.

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

Tests for !=. The default implementation is almost always sufficient, and should not be overridden without very good reason.

impl Serialize for U64x2

fn serialize<S>(&self, serializer: S) -> Result<S::Ok, S::Error>

where S: Serializer,

Serialize this value into the given Serde serializer.

impl Shl<u64> for U64x2

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

Scalar Equivalent:

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

Avx2

• _mm_set_epi64x

  Instruction sequence.

• _mm_sll_epi64

  • PSLLQ xmm, xmm

type Output = U64x2

The resulting type after applying the << operator.

impl Shl for U64x2

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

Scalar Equivalent:

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

Avx2

• _mm_sllv_epi64

  • VPSLLVQ xmm, xmm, xmm

type Output = U64x2

The resulting type after applying the << operator.

impl ShlAssign<u64> for U64x2

fn shl_assign(&mut self, amount: u64)

Performs the <<= operation.

impl ShlAssign for U64x2

fn shl_assign(&mut self, amount: U64x2)

Performs the <<= operation.

impl Shr<u64> for U64x2

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

Scalar Equivalent:

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

Avx2

• _mm_set_epi64x

  Instruction sequence.

• _mm_srl_epi64

  • PSRLQ xmm, xmm

type Output = U64x2

The resulting type after applying the >> operator.

impl Shr for U64x2

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

Scalar Equivalent:

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

Avx2

• _mm_srlv_epi64

  • VPSRLVQ xmm, xmm, xmm

type Output = U64x2

The resulting type after applying the >> operator.

impl ShrAssign<u64> for U64x2

fn shr_assign(&mut self, amount: u64)

Performs the >>= operation.

impl ShrAssign for U64x2

fn shr_assign(&mut self, amount: U64x2)

Performs the >>= operation.

impl SimdBase for U64x2

fn is_zero(&self) -> bool

Scalar Equivalent:

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

Avx2

• _mm_testz_si128

  • PTEST xmm, xmm

fn set_lo(scalar: u64) -> U64x2

Scalar Equivalent:

let mut out = [0; 2];
out[0] = scalar;
U64x2::from(out)

Avx2

• _mm_set_epi64x

  Instruction sequence.

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

Scalar Equivalent:

self.as_array()[I]

Avx2

• _mm_extract_epi64

  • PEXTRQ r64, xmm, imm8

fn broadcast(scalar: u64) -> U64x2

Scalar Equivalent:

U64x2::from([scalar; 2])

Avx2

• _mm_set1_epi64x

  Instruction sequence.

fn broadcast_lo(vector: U64x2) -> U64x2

Scalar Equivalent:

U64x2::from([vector.as_array()[0]; 2])

Avx2

• _mm_broadcastq_epi64

  • VPBROADCASTQ xmm, xmm

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

Scalar Equivalent:

U64x2::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 },
])

Avx2

• _mm_cmpeq_epi64

  • PCMPEQQ xmm, xmm

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

Scalar Equivalent:

U64x2::from([
    self.as_array()[0] & (!other.as_array()[0]),
    self.as_array()[1] & (!other.as_array()[1]),
])

Avx2

• _mm_andnot_si128

  • PANDN xmm, xmm

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

Scalar Equivalent:

U64x2::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 },
])

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(I64x2::from(*self ^ sign_bit).cmp_gt(
    I64x2::from(other ^ sign_bit)
))

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

Scalar Equivalent:

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

Avx2

• _mm_slli_epi64

  • PSLLQ xmm, imm8

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

Scalar Equivalent:

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

Avx2

• _mm_srli_epi64

  • PSRLQ xmm, imm8

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

Scalar Equivalent:

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

Avx2

• _mm_unpacklo_epi64

  • PUNPCKLQDQ xmm, xmm

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

Scalar Equivalent:

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

Avx2

• _mm_unpackhi_epi64

  • PUNPCKHQDQ xmm, xmm

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

Scalar Equivalent:

U64x2::from([
    self.as_array()[0].max(other.as_array()[0]),
    self.as_array()[1].max(other.as_array()[1]),
])

Avx2

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

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

Scalar Equivalent:

U64x2::from([
    self.as_array()[0].min(other.as_array()[0]),
    self.as_array()[1].min(other.as_array()[1]),
])

Avx2

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

const LANES: usize = 2usize

The number of elements of this vector.

const ZERO: Self

A vector where every element is zero.

type Scalar = u64

The scalar that this value holds.

type Array = [u64; 2]

The equivalent array type of this vector.

type Signed = I64x2

The signed version of this vector.

type Unsigned = U64x2

The unsigned version of this vector.

type BroadcastLoInput = U64x2

A vector of [Self::Scalar; 128 / (8 * std::mem::size_of::<Self::Scalar>())]

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

Convert the vector to an array.

impl SimdBase64 for U64x2

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

Scalar Equivalent:

U64x2::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),
])

Avx2

• _mm_mul_epu32

  • PMULUDQ xmm, xmm

impl SimdBaseGatherable<I64x2> for U64x2

Safety

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

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

Scalar Equivalent:

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

Avx2

• _mm_i64gather_epi64

  • VPGATHERQQ xmm, vm64x, xmm

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

Scalar Equivalent:

U64x2::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]
    },
])

Avx2

• _mm_mask_i64gather_epi64

  • VPGATHERQQ xmm, vm64x, xmm

impl SimdBaseGatherable<U64x2> for I64x2

Safety

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

unsafe fn gather(base: *const i64, indices: U64x2) -> I64x2

Scalar Equivalent:

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

Avx2

• _mm_i64gather_epi64

  • VPGATHERQQ xmm, vm64x, xmm

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

Scalar Equivalent:

I64x2::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]
    },
])

Avx2

• _mm_mask_i64gather_epi64

  • VPGATHERQQ xmm, vm64x, xmm

impl SimdBaseGatherable<U64x2> for U64x2

Safety

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

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

Scalar Equivalent:

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

Avx2

• _mm_i64gather_epi64

  • VPGATHERQQ xmm, vm64x, xmm

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

Scalar Equivalent:

U64x2::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]
    },
])

Avx2

• _mm_mask_i64gather_epi64

  • VPGATHERQQ xmm, vm64x, xmm

impl Sub for U64x2

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

Perform a pairwise wrapping_sub

Scalar Equivalent

U64x2::from([
    self.as_array()[0].wrapping_sub(rhs.as_array()[0]),
    self.as_array()[1].wrapping_sub(rhs.as_array()[1]),
])

AVX2 Intrinsics Used

• _mm_sub_epi64
  • PSUBQ xmm, xmm

Neon Intrinsics Used

• vsubq_u64
  • This intrinsic compiles to the following instructions:
    • SUB Vd.2D,Vn.2D,Vm.2D

type Output = U64x2

The resulting type after applying the - operator.

impl SubAssign for U64x2

fn sub_assign(&mut self, other: U64x2)

Performs the -= operation.

impl Zeroable for U64x2

fn zeroed() -> Self

Calls zeroed.

impl Copy for U64x2

impl Eq for U64x2

impl Pod for U64x2