From 7b0bc27dbbfb468fb4f2e3aff13548e6fdd64fdc Mon Sep 17 00:00:00 2001 From: elenago Date: Wed, 20 Sep 2017 13:54:28 +0200 Subject: [PATCH] Additional VMK check compliant with BitLocker standard according to: http://jessekornblum.com/publications/di09.pdf and https://github.com/libyal/libbde --- CUDA_version/cuda_attack.cu | 2 ++ OpenCL_version/kernel_attack.cl | 2 ++ 2 files changed, 4 insertions(+) diff --git a/CUDA_version/cuda_attack.cu b/CUDA_version/cuda_attack.cu index 0119e99..cdad1f2 100755 --- a/CUDA_version/cuda_attack.cu +++ b/CUDA_version/cuda_attack.cu @@ -1167,6 +1167,8 @@ __global__ void decrypt_vmk(int numStream, int tot_psw_kernel, int *found, unsig if ( ((vmkKey[0] ^ ((uint8_t) schedule4)) == 0x2c) && ((vmkKey[1] ^ ((uint8_t) (schedule4 >> 8))) == 0x00) && + ((vmkKey[4] ^ ((uint8_t) schedule5)) == 0x01) && + ((vmkKey[5] ^ ((uint8_t) (schedule5 >> 8))) == 0x00) && ((vmkKey[9] ^ ((uint8_t) (schedule6 >> 8))) == 0x20) ) { diff --git a/OpenCL_version/kernel_attack.cl b/OpenCL_version/kernel_attack.cl index d6d64fb..f4f4480 100755 --- a/OpenCL_version/kernel_attack.cl +++ b/OpenCL_version/kernel_attack.cl @@ -1114,6 +1114,8 @@ __kernel void opencl_bitcracker_attack(int numPassword, __global unsigned char * if ( ((vmkKey[0] ^ ((unsigned char) schedule4)) == 0x2c) && ((vmkKey[1] ^ ((unsigned char) (schedule4 >> 8))) == 0x00) && + ((vmkKey[4] ^ ((unsigned char) schedule5)) == 0x01) && + ((vmkKey[5] ^ ((unsigned char) (schedule5 >> 8))) == 0x00) && #if STRICT_CHECK == 1 ((vmkKey[8] ^ ((unsigned char) schedule6)) == 0x03) && #else