[PATCH] D88398: [X86] Support Intel Key Locker

[Xiang Zhang via Phabricator via llvm-commits]

xiangzhangllvm created this revision.
xiangzhangllvm added reviewers: craig.topper, LuoYuanke, annita.zhang, pengfei, MaskRay.
Herald added subscribers: llvm-commits, dang, jfb, hiraditya, mgorny.
Herald added a project: LLVM.
xiangzhangllvm requested review of this revision.

Key Locker provides a mechanism to encrypt and decrypt data with an AES key without having access
to the raw key value by converting AES keys into “handles”. These handles can be used to perform the
same encryption and decryption operations as the original AES keys, but they only work on the current
system and only until they are revoked. If software revokes Key Locker handles (e.g., on a reboot),
then any previous handles can no longer be used.


https://reviews.llvm.org/D88398

Files:
  clang/include/clang/Basic/BuiltinsX86.def
  clang/include/clang/Driver/Options.td
  clang/lib/Basic/Targets/X86.cpp
  clang/lib/Basic/Targets/X86.h
  clang/lib/CodeGen/CGBuiltin.cpp
  clang/lib/Headers/CMakeLists.txt
  clang/lib/Headers/immintrin.h
  clang/lib/Headers/keylocker_wide_intrin.h
  clang/lib/Headers/keylockerintrin.h
  clang/test/CodeGen/X86/keylocker.c
  clang/test/CodeGen/attr-target-x86.c
  clang/test/Driver/x86-target-features.c
  clang/test/Preprocessor/x86_target_features.c
  llvm/include/llvm/IR/IntrinsicsX86.td
  llvm/include/llvm/Support/X86TargetParser.def
  llvm/lib/IR/Function.cpp
  llvm/lib/Support/Host.cpp
  llvm/lib/Support/X86TargetParser.cpp
  llvm/lib/Target/X86/X86.td
  llvm/lib/Target/X86/X86ISelLowering.cpp
  llvm/lib/Target/X86/X86InstrInfo.td
  llvm/lib/Target/X86/X86InstrInfo.td.rej
  llvm/lib/Target/X86/X86InstrKL.td
  llvm/lib/Target/X86/X86Subtarget.h
  llvm/test/CodeGen/X86/keylocker-intrinsics.ll
  llvm/test/MC/Disassembler/X86/KEYLOCKER/Keylocker-x86-32-att.txt
  llvm/test/MC/Disassembler/X86/KEYLOCKER/Keylocker-x86-32-intel.txt
  llvm/test/MC/Disassembler/X86/KEYLOCKER/Keylocker-x86-64-att.txt
  llvm/test/MC/Disassembler/X86/KEYLOCKER/Keylocker-x86-64-intel.txt
  llvm/test/MC/X86/KEYLOCKER/keylocker-att.s
  llvm/test/MC/X86/KEYLOCKER/keylocker-intel.s
  llvm/test/MC/X86/KEYLOCKER/x86-64-keylocker-att.s
  llvm/test/MC/X86/KEYLOCKER/x86-64-keylocker-intel.s
  llvm/utils/TableGen/IntrinsicEmitter.cpp

-------------- next part --------------
A non-text attachment was scrubbed...
Name: D88398.294631.patch
Type: text/x-patch
Size: 146414 bytes
Desc: not available
URL: <http://lists.llvm.org/pipermail/llvm-commits/attachments/20200928/b21e3217/attachment-0001.bin>