Trait zerocopy::FromBytes

source ·
pub unsafe trait FromBytes: FromZeroes {
    // Provided methods
    fn read_from(bytes: &[u8]) -> Option<Self>
       where Self: Sized { ... }
    fn read_from_prefix(bytes: &[u8]) -> Option<Self>
       where Self: Sized { ... }
    fn read_from_suffix(bytes: &[u8]) -> Option<Self>
       where Self: Sized { ... }
}
Expand description

Types for which any byte pattern is valid.

WARNING: Do not implement this trait yourself! Instead, use #[derive(FromBytes)] (requires the derive Cargo feature).

FromBytes types can safely be deserialized from an untrusted sequence of bytes because any byte sequence corresponds to a valid instance of the type.

FromBytes is ignorant of byte order. For byte order-aware types, see the byteorder module.

Safety

This section describes what is required in order for T: FromBytes, and what unsafe code may assume of such types. #[derive(FromBytes)] only permits types which satisfy these requirements. If you don’t plan on implementing FromBytes manually, and you don’t plan on writing unsafe code that operates on FromBytes types, then you don’t need to read this section.

If T: FromBytes, then unsafe code may assume that:

  • It is sound to treat any initialized sequence of bytes of length size_of::<T>() as a T.
  • Given b: &[u8] where b.len() == size_of::<T>() and b is aligned to align_of::<T>(), it is sound to construct a t: &T at the same address as b, and it is sound for both b and t to be live at the same time.

If a type is marked as FromBytes which violates this contract, it may cause undefined behavior.

If a type has the following properties, then it is sound to implement FromBytes for that type:

  • If the type is a struct, all of its fields must satisfy the requirements to be FromBytes (they do not actually have to be FromBytes)
  • If the type is an enum:
    • It must be a C-like enum (meaning that all variants have no fields).
    • It must have a defined representation (reprs C, u8, u16, u32, u64, usize, i8, i16, i32, i64, or isize).
    • The maximum number of discriminants must be used (so that every possible bit pattern is a valid one). Be very careful when using the C, usize, or isize representations, as their size is platform-dependent.
  • The type must not contain any UnsafeCells (this is required in order for it to be sound to construct a &[u8] and a &T to the same region of memory). The type may contain references or pointers to UnsafeCells so long as those values can themselves be initialized from zeroes (FromBytes is not currently implemented for, e.g., Option<*const UnsafeCell<_>>, but it could be one day).

Rationale

Why isn’t an explicit representation required for structs?

Per the Rust reference,

The representation of a type can change the padding between fields, but does not change the layout of the fields themselves.

Since the layout of structs only consists of padding bytes and field bytes, a struct is soundly FromBytes if:

  1. its padding is soundly FromBytes, and
  2. its fields are soundly FromBytes.

The answer to the first question is always yes: padding bytes do not have any validity constraints. A discussion of this question in the Unsafe Code Guidelines Working Group concluded that it would be virtually unimaginable for future versions of rustc to add validity constraints to padding bytes.

Whether a struct is soundly FromBytes therefore solely depends on whether its fields are FromBytes.

Provided Methods§

source

fn read_from(bytes: &[u8]) -> Option<Self>
where Self: Sized,

Reads a copy of Self from bytes.

If bytes.len() != size_of::<Self>(), read_from returns None.

source

fn read_from_prefix(bytes: &[u8]) -> Option<Self>
where Self: Sized,

Reads a copy of Self from the prefix of bytes.

read_from_prefix reads a Self from the first size_of::<Self>() bytes of bytes. If bytes.len() < size_of::<Self>(), it returns None.

source

fn read_from_suffix(bytes: &[u8]) -> Option<Self>
where Self: Sized,

Reads a copy of Self from the suffix of bytes.

read_from_suffix reads a Self from the last size_of::<Self>() bytes of bytes. If bytes.len() < size_of::<Self>(), it returns None.

Implementations on Foreign Types§

source§

impl FromBytes for Option<NonZeroI8>

source§

impl FromBytes for Option<NonZeroI16>

source§

impl FromBytes for Option<NonZeroI32>

source§

impl FromBytes for Option<NonZeroI64>

source§

impl FromBytes for Option<NonZeroI128>

source§

impl FromBytes for Option<NonZeroIsize>

source§

impl FromBytes for Option<NonZeroU8>

source§

impl FromBytes for Option<NonZeroU16>

source§

impl FromBytes for Option<NonZeroU32>

source§

impl FromBytes for Option<NonZeroU64>

source§

impl FromBytes for Option<NonZeroU128>

source§

impl FromBytes for Option<NonZeroUsize>

source§

impl FromBytes for f32

source§

impl FromBytes for f64

source§

impl FromBytes for i8

source§

impl FromBytes for i16

source§

impl FromBytes for i32

source§

impl FromBytes for i64

source§

impl FromBytes for i128

source§

impl FromBytes for isize

source§

impl FromBytes for u8

source§

impl FromBytes for u16

source§

impl FromBytes for u32

source§

impl FromBytes for u64

source§

impl FromBytes for u128

source§

impl FromBytes for ()

source§

impl FromBytes for usize

source§

impl FromBytes for __m128

source§

impl FromBytes for __m128d

source§

impl FromBytes for __m128i

source§

impl FromBytes for __m256

source§

impl FromBytes for __m256d

source§

impl FromBytes for __m256i

source§

impl<T: FromBytes> FromBytes for [T]

source§

impl<T: FromBytes> FromBytes for Wrapping<T>

source§

impl<T: FromBytes> FromBytes for MaybeUninit<T>

source§

impl<T: ?Sized + FromBytes> FromBytes for ManuallyDrop<T>

source§

impl<T: ?Sized> FromBytes for PhantomData<T>

source§

impl<const N: usize, T: FromBytes> FromBytes for [T; N]

Implementors§

source§

impl<O> FromBytes for F32<O>

source§

impl<O> FromBytes for F64<O>

source§

impl<O> FromBytes for I16<O>

source§

impl<O> FromBytes for I32<O>

source§

impl<O> FromBytes for I64<O>

source§

impl<O> FromBytes for I128<O>

source§

impl<O> FromBytes for U16<O>

source§

impl<O> FromBytes for U32<O>

source§

impl<O> FromBytes for U64<O>

source§

impl<O> FromBytes for U128<O>

source§

impl<T> FromBytes for Unalign<T>
where T: FromBytes,