aes 0.9.0

Pure Rust implementation of the Advanced Encryption Standard (a.k.a. Rijndael)
Documentation 
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85

#![allow(unsafe_op_in_unsafe_fn)]

use crate::x86::{Block64, Simd128RoundKeys, Simd512RoundKeys, arch::*};
use cipher::inout::InOut;
use core::mem::MaybeUninit;

#[target_feature(enable = "avx512f")]
#[inline]
pub(crate) unsafe fn broadcast_keys<const KEYS: usize>(
    keys: &Simd128RoundKeys<KEYS>,
) -> Simd512RoundKeys<KEYS> {
    keys.map(|key| _mm512_broadcast_i32x4(key))
}

#[target_feature(enable = "avx512f,vaes")]
#[inline]
pub(crate) unsafe fn encrypt64<const KEYS: usize>(
    keys: &Simd512RoundKeys<KEYS>,
    blocks: InOut<'_, '_, Block64>,
) {
    assert!(KEYS == 11 || KEYS == 13 || KEYS == 15);

    let (iptr, optr) = blocks.into_raw();
    let iptr = iptr.cast::<__m512i>();
    let optr = optr.cast::<__m512i>();

    let mut data: [MaybeUninit<__m512i>; 16] = MaybeUninit::uninit().assume_init();

    (0..16).for_each(|i| {
        data[i].write(iptr.add(i).read_unaligned());
    });
    let mut data: [__m512i; 16] = unsafe { ::core::mem::transmute(data) };

    for vec in &mut data {
        *vec = _mm512_xor_si512(*vec, keys[0]);
    }
    for key in &keys[1..KEYS - 1] {
        for vec in &mut data {
            *vec = _mm512_aesenc_epi128(*vec, *key);
        }
    }
    for vec in &mut data {
        *vec = _mm512_aesenclast_epi128(*vec, keys[KEYS - 1]);
    }

    (0..16).for_each(|i| {
        optr.add(i).write_unaligned(data[i]);
    });
}

#[target_feature(enable = "avx512f,vaes")]
#[inline]
pub(crate) unsafe fn decrypt64<const KEYS: usize>(
    keys: &Simd512RoundKeys<KEYS>,
    blocks: InOut<'_, '_, Block64>,
) {
    assert!(KEYS == 11 || KEYS == 13 || KEYS == 15);

    let (iptr, optr) = blocks.into_raw();
    let iptr = iptr.cast::<__m512i>();
    let optr = optr.cast::<__m512i>();

    let mut data: [MaybeUninit<__m512i>; 16] = MaybeUninit::uninit().assume_init();

    (0..16).for_each(|i| {
        data[i].write(iptr.add(i).read_unaligned());
    });
    let mut data: [__m512i; 16] = unsafe { ::core::mem::transmute(data) };

    for vec in &mut data {
        *vec = _mm512_xor_si512(*vec, keys[0]);
    }
    for key in &keys[1..KEYS - 1] {
        for vec in &mut data {
            *vec = _mm512_aesdec_epi128(*vec, *key);
        }
    }
    for vec in &mut data {
        *vec = _mm512_aesdeclast_epi128(*vec, keys[KEYS - 1]);
    }

    (0..16).for_each(|i| {
        optr.add(i).write_unaligned(data[i]);
    });
}