Struct U4 

#[repr(transparent)]
pub struct U4(pub u8);

Unsigned 4-bit integer element marker — packed-pair storage.

#[repr(transparent)] around u8. Packing convention is identical to S4 (low nibble = even index, high nibble = odd index); the only difference is zero-extension to s32 on the GPU side (nibble & 0xF).

Numerical range per element: [0, 15]. Plan-layer conventions (M/N/K in elements, LDs in storage slots, K even) match S4. Routes through Ada Lovelace int4 tensor cores (mma.sync.aligned.m16n8k64.row.col.satfinite.s32.u4.u4.s32) with the same S32 accumulator and float α/β family as S4.

Tuple Fields

0: u8

Implementations

impl U4

pub fn pack(lo: u8, hi: u8) -> U4

Pack two u4 values [lo, hi] (each in [0, 15]) into one storage slot. Values outside the range are masked to their low 4 bits.

pub fn unpack(self) -> [u8; 2]

Unpack into [low_nibble, high_nibble]. Each returned value is in [0, 15].

Trait Implementations

impl Clone for U4

fn clone(&self) -> U4

Returns a duplicate of the value.

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

Performs copy-assignment from source.

impl Copy for U4

impl Debug for U4

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

Formats the value using the given formatter.

impl Default for U4

fn default() -> U4

Returns the “default value” for a type.

impl DeviceRepr for U4

impl Eq for U4

impl Hash for U4

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

where __H: Hasher,

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 IntElement for U4

impl KernelDtype for U4

const KIND: ElementKind = ElementKind::U4

Runtime tag for this dtype. Stable across the workspace — keyed by this same enum in crate::KernelSku::element.

impl Ord for U4

fn cmp(&self, other: &U4) -> Ordering

This method returns an Ordering between self and other.

fn max(self, other: Self) -> Self

where Self: Sized,

Compares and returns the maximum of two values.

fn min(self, other: Self) -> Self

where Self: Sized,

Compares and returns the minimum of two values.

fn clamp(self, min: Self, max: Self) -> Self

where Self: Sized,

Restrict a value to a certain interval.

impl PartialEq for U4

fn eq(&self, other: &U4) -> 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 PartialOrd for U4

fn partial_cmp(&self, other: &U4) -> Option<Ordering>

This method returns an ordering between self and other values if one exists.

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

Tests less than (for self and other) and is used by the < operator.

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

Tests less than or equal to (for self and other) and is used by the <= operator.

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

Tests greater than (for self and other) and is used by the > operator.

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

Tests greater than or equal to (for self and other) and is used by the >= operator.

impl StructuralPartialEq for U4