Trait uefi_std::marker::Unpin

#[lang = "unpin"]pub auto trait Unpin { }

Types that can be safely moved after being pinned.

Rust itself has no notion of immovable types, and considers moves (e.g., through assignment or mem::replace) to always be safe.

The Pin type is used instead to prevent moves through the type system. Pointers P<T> wrapped in the Pin<P<T>> wrapper can't be moved out of. See the pin module documentation for more information on pinning.

Implementing the Unpin trait for T lifts the restrictions of pinning off the type, which then allows moving T out of Pin<P<T>> with functions such as mem::replace.

Unpin has no consequence at all for non-pinned data. In particular, mem::replace happily moves !Unpin data (it works for any &mut T, not just when T: Unpin). However, you cannot use mem::replace on data wrapped inside a Pin<P<T>> because you cannot get the &mut T you need for that, and that is what makes this system work.

So this, for example, can only be done on types implementing Unpin:

use std::mem;
use std::pin::Pin;

let mut string = "this".to_string();
let mut pinned_string = Pin::new(&mut string);

// We need a mutable reference to call `mem::replace`.
// We can obtain such a reference by (implicitly) invoking `Pin::deref_mut`,
// but that is only possible because `String` implements `Unpin`.
mem::replace(&mut *pinned_string, "other".to_string());

This trait is automatically implemented for almost every type.

Implementations on Foreign Types

impl Unpin for Argument

impl Unpin for FormatSpec

impl Unpin for Alignment

impl Unpin for Count

impl<T> Unpin for Ready<T>

impl Unpin for Waker

impl<F> Unpin for PollFn<F>

impl<T> Unpin for Pending<T>

impl<T> Unpin for Arc<T> where
    T: ?Sized, 

Loading content...

Implementors

impl !Unpin for PhantomPinned

impl<'a, T> Unpin for &'a T where
    T: 'a + ?Sized, 

impl<'a, T> Unpin for &'a mut T where
    T: 'a + ?Sized, 

impl<T> Unpin for *const T where
    T: ?Sized, 

impl<T> Unpin for *mut T where
    T: ?Sized, 

impl<T> Unpin for Rc<T> where
    T: ?Sized, 

impl<T, A> Unpin for Box<T, A> where
    A: Allocator + 'static,
    T: ?Sized, 

Loading content...

Auto implementors

impl Unpin for Ordering

impl Unpin for Infallible

impl Unpin for uefi_std::fmt::Alignment

impl Unpin for SearchStep

impl Unpin for TypeId

impl Unpin for CpuidResult

impl Unpin for __m128

impl Unpin for __m128d

impl Unpin for __m128i

impl Unpin for __m256

impl Unpin for __m256d

impl Unpin for __m256i

impl Unpin for __m512

impl Unpin for __m512d

impl Unpin for __m512i

impl Unpin for TryFromSliceError

impl Unpin for BorrowError

impl Unpin for BorrowMutError

impl Unpin for CharTryFromError

impl Unpin for DecodeUtf16Error

impl Unpin for uefi_std::char::EscapeDebug

impl Unpin for uefi_std::char::EscapeDefault

impl Unpin for uefi_std::char::EscapeUnicode

impl Unpin for ParseCharError

impl Unpin for ToLowercase

impl Unpin for ToUppercase

impl Unpin for Error

impl Unpin for Dir

impl Unpin for File

impl Unpin for FileSystem

impl Unpin for SipHasher

impl Unpin for Stdout

impl Unpin for LoadedImage

impl Unpin for RangeFull

impl Unpin for NoneError

impl Unpin for Pointer

impl Unpin for TraitObject

impl Unpin for Shell

impl Unpin for ParseBoolError

impl Unpin for Utf8Error

impl Unpin for FromUtf8Error

impl Unpin for FromUtf16Error

impl Unpin for String

impl Unpin for [u8]

impl Unpin for bool

impl Unpin for char

impl Unpin for f32

impl Unpin for f64

impl Unpin for i8

impl Unpin for i16

impl Unpin for i32

impl Unpin for i64

impl Unpin for i128

impl Unpin for isize

impl Unpin for str

impl Unpin for u8

impl Unpin for u16

impl Unpin for u32

impl Unpin for u64

impl Unpin for u128

impl Unpin for usize

impl<'a> Unpin for Arguments<'a>

impl<'a> Unpin for Formatter<'a>

impl<'a> Unpin for CharSearcher<'a>

impl<'a> Unpin for Bytes<'a>

impl<'a> Unpin for CharIndices<'a>

impl<'a> Unpin for Chars<'a>

impl<'a> Unpin for EncodeUtf16<'a>

impl<'a> Unpin for uefi_std::str::EscapeDebug<'a>

impl<'a> Unpin for uefi_std::str::EscapeDefault<'a>

impl<'a> Unpin for uefi_std::str::EscapeUnicode<'a>

impl<'a> Unpin for Lines<'a>

impl<'a> Unpin for LinesAny<'a>

impl<'a> Unpin for SplitAsciiWhitespace<'a>

impl<'a> Unpin for SplitWhitespace<'a>

impl<'a> Unpin for uefi_std::string::Drain<'a>

impl<'a, 'b> Unpin for DebugList<'a, 'b> where
    'b: 'a, 

impl<'a, 'b> Unpin for DebugMap<'a, 'b> where
    'b: 'a, 

impl<'a, 'b> Unpin for DebugSet<'a, 'b> where
    'b: 'a, 

impl<'a, 'b> Unpin for DebugStruct<'a, 'b> where
    'b: 'a, 

impl<'a, 'b> Unpin for DebugTuple<'a, 'b> where
    'b: 'a, 

impl<'a, 'b> Unpin for CharSliceSearcher<'a, 'b>

impl<'a, 'b> Unpin for StrSearcher<'a, 'b>

impl<'a, A> Unpin for uefi_std::option::Iter<'a, A>

impl<'a, A> Unpin for uefi_std::option::IterMut<'a, A>

impl<'a, B: ?Sized> Unpin for Cow<'a, B> where
    <B as ToOwned>::Owned: Unpin, 

impl<'a, F> Unpin for CharPredicateSearcher<'a, F> where
    F: MultiCharEq + Unpin, 

impl<'a, I, A> Unpin for Splice<'a, I, A> where
    I: Unpin, 

impl<'a, P> Unpin for MatchIndices<'a, P> where
    <P as Pattern<'a>>::Searcher: Unpin, 

impl<'a, P> Unpin for Matches<'a, P> where
    <P as Pattern<'a>>::Searcher: Unpin, 

impl<'a, P> Unpin for RMatchIndices<'a, P> where
    <P as Pattern<'a>>::Searcher: Unpin, 

impl<'a, P> Unpin for RMatches<'a, P> where
    <P as Pattern<'a>>::Searcher: Unpin, 

impl<'a, P> Unpin for uefi_std::str::RSplit<'a, P> where
    <P as Pattern<'a>>::Searcher: Unpin, 

impl<'a, P> Unpin for uefi_std::str::RSplitN<'a, P> where
    <P as Pattern<'a>>::Searcher: Unpin, 

impl<'a, P> Unpin for RSplitTerminator<'a, P> where
    <P as Pattern<'a>>::Searcher: Unpin, 

impl<'a, P> Unpin for uefi_std::str::Split<'a, P> where
    <P as Pattern<'a>>::Searcher: Unpin, 

impl<'a, P> Unpin for uefi_std::str::SplitN<'a, P> where
    <P as Pattern<'a>>::Searcher: Unpin, 

impl<'a, P> Unpin for SplitTerminator<'a, P> where
    <P as Pattern<'a>>::Searcher: Unpin, 

impl<'a, T> Unpin for uefi_std::result::Iter<'a, T>

impl<'a, T> Unpin for uefi_std::result::IterMut<'a, T>

impl<'a, T> Unpin for Chunks<'a, T>

impl<'a, T> Unpin for ChunksExact<'a, T>

impl<'a, T> Unpin for ChunksExactMut<'a, T>

impl<'a, T> Unpin for ChunksMut<'a, T>

impl<'a, T> Unpin for uefi_std::slice::Iter<'a, T>

impl<'a, T> Unpin for uefi_std::slice::IterMut<'a, T>

impl<'a, T> Unpin for RChunks<'a, T>

impl<'a, T> Unpin for RChunksExact<'a, T>

impl<'a, T> Unpin for RChunksExactMut<'a, T>

impl<'a, T> Unpin for RChunksMut<'a, T>

impl<'a, T> Unpin for Windows<'a, T>

impl<'a, T, A> Unpin for uefi_std::vec::Drain<'a, T, A>

impl<'a, T, F, A> Unpin for DrainFilter<'a, T, F, A> where
    F: Unpin, 

impl<'a, T, P> Unpin for uefi_std::slice::RSplit<'a, T, P> where
    P: Unpin, 

impl<'a, T, P> Unpin for RSplitMut<'a, T, P> where
    P: Unpin, 

impl<'a, T, P> Unpin for uefi_std::slice::RSplitN<'a, T, P> where
    P: Unpin, 

impl<'a, T, P> Unpin for RSplitNMut<'a, T, P> where
    P: Unpin, 

impl<'a, T, P> Unpin for uefi_std::slice::Split<'a, T, P> where
    P: Unpin, 

impl<'a, T, P> Unpin for SplitMut<'a, T, P> where
    P: Unpin, 

impl<'a, T, P> Unpin for uefi_std::slice::SplitN<'a, T, P> where
    P: Unpin, 

impl<'a, T, P> Unpin for SplitNMut<'a, T, P> where
    P: Unpin, 

impl<'a, T, const N: usize> Unpin for ArrayChunks<'a, T, N>

impl<'a, T, const N: usize> Unpin for ArrayChunksMut<'a, T, N>

impl<'a, T, const N: usize> Unpin for ArrayWindows<'a, T, N>

impl<'b, T: ?Sized> Unpin for Ref<'b, T>

impl<'b, T: ?Sized> Unpin for RefMut<'b, T>

impl<A> Unpin for Repeat<A> where
    A: Unpin, 

impl<A> Unpin for uefi_std::option::IntoIter<A> where
    A: Unpin, 

impl<A, B> Unpin for Chain<A, B> where
    A: Unpin,
    B: Unpin, 

impl<A, B> Unpin for Zip<A, B> where
    A: Unpin,
    B: Unpin, 

impl<B, C> Unpin for ControlFlow<B, C> where
    B: Unpin,
    C: Unpin, 

impl<F> Unpin for FromFn<F> where
    F: Unpin, 

impl<F> Unpin for OnceWith<F> where
    F: Unpin, 

impl<F> Unpin for RepeatWith<F> where
    F: Unpin, 

impl<H> Unpin for BuildHasherDefault<H> where
    H: Unpin, 

impl<I> Unpin for DecodeUtf16<I> where
    I: Unpin, 

impl<I> Unpin for Cloned<I> where
    I: Unpin, 

impl<I> Unpin for Copied<I> where
    I: Unpin, 

impl<I> Unpin for Cycle<I> where
    I: Unpin, 

impl<I> Unpin for Enumerate<I> where
    I: Unpin, 

impl<I> Unpin for Flatten<I> where
    I: Unpin,
    <<I as Iterator>::Item as IntoIterator>::IntoIter: Unpin, 

impl<I> Unpin for Fuse<I> where
    I: Unpin, 

impl<I> Unpin for Peekable<I> where
    I: Unpin,
    <I as Iterator>::Item: Unpin, 

impl<I> Unpin for Skip<I> where
    I: Unpin, 

impl<I> Unpin for StepBy<I> where
    I: Unpin, 

impl<I> Unpin for Take<I> where
    I: Unpin, 

impl<I, F> Unpin for FilterMap<I, F> where
    F: Unpin,
    I: Unpin, 

impl<I, F> Unpin for Inspect<I, F> where
    F: Unpin,
    I: Unpin, 

impl<I, F> Unpin for Map<I, F> where
    F: Unpin,
    I: Unpin, 

impl<I, P> Unpin for Filter<I, P> where
    I: Unpin,
    P: Unpin, 

impl<I, P> Unpin for MapWhile<I, P> where
    I: Unpin,
    P: Unpin, 

impl<I, P> Unpin for SkipWhile<I, P> where
    I: Unpin,
    P: Unpin, 

impl<I, P> Unpin for TakeWhile<I, P> where
    I: Unpin,
    P: Unpin, 

impl<I, St, F> Unpin for Scan<I, St, F> where
    F: Unpin,
    I: Unpin,
    St: Unpin, 

impl<I, U, F> Unpin for FlatMap<I, U, F> where
    F: Unpin,
    I: Unpin,
    <U as IntoIterator>::IntoIter: Unpin, 

impl<Idx> Unpin for Range<Idx> where
    Idx: Unpin, 

impl<Idx> Unpin for RangeFrom<Idx> where
    Idx: Unpin, 

impl<Idx> Unpin for RangeInclusive<Idx> where
    Idx: Unpin, 

impl<Idx> Unpin for RangeTo<Idx> where
    Idx: Unpin, 

impl<Idx> Unpin for RangeToInclusive<Idx> where
    Idx: Unpin, 

impl<P> Unpin for Pin<P> where
    P: Unpin, 

impl<T> Unpin for Bound<T> where
    T: Unpin, 

impl<T> Unpin for Option<T> where
    T: Unpin, 

impl<T> Unpin for Reverse<T> where
    T: Unpin, 

impl<T> Unpin for Empty<T> where
    T: Unpin, 

impl<T> Unpin for Once<T> where
    T: Unpin, 

impl<T> Unpin for Rev<T> where
    T: Unpin, 

impl<T> Unpin for Discriminant<T> where
    <T as DiscriminantKind>::Discriminant: Unpin, 

impl<T> Unpin for uefi_std::result::IntoIter<T> where
    T: Unpin, 

impl<T> Unpin for MaybeUninit<T> where
    T: Unpin, 

impl<T> Unpin for [T] where
    T: Unpin, 

impl<T, A> Unpin for uefi_std::vec::IntoIter<T, A> where
    A: Unpin,
    T: Unpin, 

impl<T, A> Unpin for Vec<T, A> where
    A: Unpin,
    T: Unpin, 

impl<T, E> Unpin for Result<T, E> where
    E: Unpin,
    T: Unpin, 

impl<T, F> Unpin for Successors<T, F> where
    F: Unpin,
    T: Unpin, 

impl<T, const N: usize> Unpin for uefi_std::array::IntoIter<T, N> where
    T: Unpin, 

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

impl<T: ?Sized> Unpin for Cell<T> where
    T: Unpin, 

impl<T: ?Sized> Unpin for RefCell<T> where
    T: Unpin, 

impl<T: ?Sized> Unpin for UnsafeCell<T> where
    T: Unpin, 

impl<T: ?Sized> Unpin for PhantomData<T> where
    T: Unpin, 

impl<T: ?Sized> Unpin for ManuallyDrop<T> where
    T: Unpin, 

impl<T: ?Sized> Unpin for NonNull<T>

impl<T: ?Sized> Unpin for Weak<T>

impl<Y, R> Unpin for GeneratorState<Y, R> where
    R: Unpin,
    Y: Unpin, 

Loading content...