Commit Graph

3245 Commits (d71afd6d7a3aa0fb2c7a832ed2adf2f65dc2b504)

Author SHA1 Message Date
vlo 84b8a1b1eb Suggested changes for pull request
5 years ago
Jens Steube ce8a6fde0a Fix status screen current password query
5 years ago
Jens Steube f84eaa2e4d Fix bitsliced algorithm brute-force with CUDA
5 years ago
Sein Coray ff718cf53f
all pkzip modules use u32 to store the hash data and use appropriate printing
5 years ago
Sein Coray 2434380da2
fixed printing of hash for module 17220 and 17230 using the u32 data array
5 years ago
Sein Coray e300fe0d63
fixes to avoid crashing on gpu on multiple inner loops
5 years ago
Jens Steube f2b1dfea31
Merge pull request #2018 from Chick3nman/master
5 years ago
Jens Steube 85f7d50fb8
Merge pull request #2021 from philsmd/master
5 years ago
Sein Coray e39a9284e1
Merge remote-tracking branch 'upstream/master'
5 years ago
Sein Coray d5418c25c5
remove unused digest variable
5 years ago
Sein Coray fe61813af4
remove unused digest variable
5 years ago
Jens Steube 523e0f7151 Fix free unallocated memory in case OpenCL initialization failed
5 years ago
Jens Steube bca03bb7ed CUDA offers a nice way to query available device memory, no need to brute force
5 years ago
Jens Steube 1943c35e4a Improve kernel-loops detection for slow hashes
5 years ago
philsmd 07a1bdb12c
added support for $electrum$3 hashes (-m 16600)
5 years ago
Jens Steube fa9d073f9a Manually unroll sha2 hashes
5 years ago
Jens Steube aa8e000d31 Flag OPTS_TYPE_PREFERED_THREAD no longer needed
5 years ago
Jens Steube a6bc1d3cc0 Experimental kernel-thread autotuner
5 years ago
Jens Steube 2b0f657564 Limit some modules to 64 threads in order to get additional L1 cache
5 years ago
Jens Steube d59474fded Testwise unlock full thread count on NVidia
5 years ago
Jens Steube d378aa7ab9 Show host memory requirement on startup
5 years ago
Chick3nman 717b82c406
Add extra warning for --force
5 years ago
Jens Steube 46f737c5af Use real constant memory on CUDA
5 years ago
Sein Coray 371991e079
included speed improvements and feedback from atom applied to all 172xx kernel variants
5 years ago
Jens Steube 5d14a59304 Need 3.x nvrtc minimum
5 years ago
vlo 556db9a9e9 Fix: buffer sizes (again)
5 years ago
Jens Steube 54feb62e94 brute-force nvrtc .dll name
5 years ago
Jens Steube a2b5981303 Fix some library names
5 years ago
vlo ee500bec02 Fixed: buffer overflows
5 years ago
Sein Coray e4d8e4a7ad
bring fork up-to-date
5 years ago
Jens Steube be8f29ca39 Only warn about broken NVIDIA driver
5 years ago
Jens Steube 39e150fc1e Use xxx_v2 CUDA symbols
5 years ago
vlo 23c3e723f7 Implemeted table for alternate base64
5 years ago
Jens Steube 33028314f0 Add hc_cuCtxSetCacheConfig()
5 years ago
Jens Steube fb82bfc169 Improve thread handling based on FIXED_LOCAL_SIZE
5 years ago
Jens Steube 3a3df091c7 Fix CUDA num_elements
5 years ago
vlo 14dd1aaaeb Added support for passlib pbkdf2-sha256 and sha1
5 years ago
Jens Steube a01cc28ec6
Merge pull request #2014 from hashcat/master
5 years ago
Jens Steube 363e789b89 Assume local nvrtc.dll and cuda.dll on windows
5 years ago
philsmd f45a726376
fixes #2012: add Deflate support for 7-Zip using zlib
5 years ago
Jens Steube a7d04adba3 Fix opencl_devices_active and backend_devices_active
5 years ago
Jens Steube 8ff8c5d536 Add LOCAL_VK to make use of __shared__
5 years ago
Jens Steube bbed0cd67a Fix test.sh and bitsliced algos
5 years ago
Jens Steube d0bd33c9d1 Rename CONSTANT_AS to CONSTANT_VK
5 years ago
Jens Steube 64c495dfa5 Use CUDA stream for all cuLaunchKernel() invocations
5 years ago
Jens Steube d94f582097 Replace CEILDIV() with round_up_multiple_64()
5 years ago
Jens Steube e9c04c2446 More CUDA implementation
5 years ago
Jens Steube 08dc1acc02 More CUDA rewrites
5 years ago
Jens Steube ec9925f3b1 Warnings self-check and autotune with CUDA
5 years ago
Jens Steube 4df00033d7 Prepare CUDA events
5 years ago
Jens Steube f2948460c9 Some first kernel invocations
5 years ago
Jens Steube 5ee033673c Disable name mangling in NVRTC's PTX output and more
5 years ago
Jens Steube 503304f36a Add some first CUDA device memory allocations and host buffer copies
5 years ago
vlo 003e23bae8 Change hash mode of addition, add test module
5 years ago
Jens Steube 50a6e720ca More OpenCL variables rename
5 years ago
Jens Steube af8e317cf4 Begin renaming some OpenCL only variables
5 years ago
Jens Steube a6fa7a2749 Add support for some first CUDA module loader
5 years ago
Jens Steube 456c57a6d0 Set vector width size for CUDA
5 years ago
vlo 4510504257 New module for Python passlib pbkdf2-sha512
5 years ago
Jens Steube 3c4f4df771 Rename some more variables
5 years ago
Jens Steube 495d89f831 Find alias devices across different backend API's
5 years ago
Jens Steube 6fd936b43a Removed --opencl-platforms filter in order to force backend device numbers to stay constant
5 years ago
Jens Steube e3500ff4aa Add CUDA device attributes to -I
5 years ago
Jens Steube c80e516c3c
Merge pull request #2007 from hashcat/master
5 years ago
Jens Steube 6caa78695f Backport -m 19500 fix to -m 19300
5 years ago
Jens Steube 922fa2e351 Use md5 for generatic unique salt for salt sorter in -m 19500
5 years ago
Jens Steube d862458ab5 Begin renaming API specific variables in backend section
5 years ago
Jens Steube d73c0ac8a9 More CUDA attribute queries
6 years ago
Jens Steube a415422123 Initialize CUDA devices and some first attribute queries
6 years ago
Jens Steube 222be0b0dc
Merge pull request #2005 from hashcat/master
6 years ago
Jens Steube 200e72dba3 Limit -T maximum on -m 3200 to what's possible based on device specific shared memory available
6 years ago
Jens Steube d67de66453 Disable kernel cache on -m 3200
6 years ago
Jens Steube 58213c81d6 Add vector datatypes operators
6 years ago
Jens Steube 052e42ccef Fix CUDA_ARCH value
6 years ago
Jens Steube 06171958ee Add --gpu-architecture to NVRTC build options
6 years ago
Jens Steube 9faba41848 Use nvrtc to compile PTX (resulting PTX not yet used)
6 years ago
Jens Steube 4045e60021 Add nvrtc wrapper for later use
6 years ago
Jens Steube 4b986de5fb Prepare native CUDA hybrid integration
6 years ago
jsteube b9aaaf7809 Move 198xx DiskCryptor to 200xx to not collide with Kerberos 5, etype 17, Pre-Auth
6 years ago
Jens Steube 17ab30b29f
Merge pull request #1991 from brandoncasaba/master
6 years ago
jsteube 8b51843bb2 Mark -m 15300 and -m 1590 as unstable on AMDGPU driver
6 years ago
jsteube 926e99811c Add some more NO_UNROLL to avoid module_unstable_warnings
6 years ago
jsteube 08a74cfcb5 Add NO_UNROLL to -m 1750 for AMDGPU driver
6 years ago
jsteube ac4f8e688a Dependencies: Updated OpenCL-Headers to latest version from GitHub master repository
6 years ago
jsteube 5f3d9e08b9 Kernel Compile: Removed -cl-std= from all kernel build options since we're compatible to all OpenCL versions
6 years ago
jsteube f424dd1edb Fix tools/install_modules.sh ro uninstall pycryptodome
6 years ago
jsteube 4548d15dde Fix spin_damp datatype
6 years ago
jsteube 5b97fe7514 Workaround volatile for -m 2500 and -m 2501 for macosx
6 years ago
jsteube 6d21c1633b Fix loop_step value in selftest.c, this also workarounds Trap 6 errors
6 years ago
Jens Steube e7ae8e6863 Requirements: Update runtime check for minimum NVIDIA driver version from 367.x to 418.56 or later
6 years ago
Jens Steube 38c1029f2e Need volatile for IRIS GPU on Mac OSX for -m 2500 and -m 2501
6 years ago
Brandon Chalk 0a4ce19915 Merge branch 'master' of https://github.com/hashcat/hashcat
6 years ago
jsteube 56ae7fa2b8 Remove warnings no longer relevant in -m 15600 and -m 16300
6 years ago
jsteube e0d0721109 Workaround for Page not present or supervisor privilege JiT fail on ROCM for -m 13400
6 years ago
jsteube 8e89617015 Workaround setting password length bug in ROCM and POCL for -m 10100
6 years ago
Jens Steube 1370dc4700 Limit kernel-accel in -m 11600 to 128
6 years ago
jsteube 7c6970dbdd Remove hard-coded static keyword from OpenCL kernels
6 years ago
Jens Steube 27f130ea90 Kernel Cache: Reactivate OpenCL runtime specific kernel caches
6 years ago
Jens Steube db91876d23 Disable check for device_available_mem on Windows in combination with AMD drivers
6 years ago
philsmd 7557f884c5
outfile remove: fix hash parsing
6 years ago
jsteube fea92595a4 Filter out 8th bit in -m 1500 password characters
6 years ago
Brandon Chalk 61ac3e3282 Minor speed and readability improvements to mode 19800 and 19900
6 years ago
Brandon Chalk 95c74c52c1 Add hash modes 19800 (krb5pa etype 17) and 19900 (krb5pa etype 18)
6 years ago
jsteube 764ca0c1c6 Add hash line separator backward compatibility for -m 16800
6 years ago
jsteube 92f4ccce93 Increase buffer size for --example-hashes output
6 years ago
ZeroBeat c572c37637 prepare new hashline
6 years ago
jsteube dbd8181c15 Disable stderr temporary since OpenCL runtime JiT (LLVM) prints directly to stderr when it should not
6 years ago
jsteube 28437b0ab0 Add NV inline assembly instruction set check on startup
6 years ago
jsteube 4cd98603f5 Add DiskCryptor modules for 1024 bit and 1536 and support for Serpent and Twofish. Be careful, untested yet!
6 years ago
philsmd 60c255a69d
added -m 19800 = DiskCryptor AES
6 years ago
jsteube aed98e0795 Merge branch 'master' of https://github.com/hashcat/hashcat
6 years ago
jsteube a22483f540 Remove some misleading error message
6 years ago
jsteube 773dab9161 Mark -m 10700 as unstable on AMDGPU driver in pure kernel mode
6 years ago
jsteube d950918fe9 Fix missing module_jit_build_options() in -m 17300
6 years ago
jsteube d7286e50a7 Mode 19500 on AMDGPU driver no longer produces self-test failures
6 years ago
jsteube c911f2bd83 Fix some OpenCL JiT compiler warnings on ROCM
6 years ago
jsteube e779c22c2c Remove some warnings no longer needed
6 years ago
jsteube 3c9d26b161 Add some conditions to make scan-build happy
6 years ago
jsteube 05a38a42b7 Initialize some values to make scan-build happy
6 years ago
jsteube 2fab28a6f3 Add some useful converters
6 years ago
jsteube f374da11e3 Fix function pointer can be NULL
6 years ago
magnum 009cf26a04 Mute a -Wformat warning and fix some whitespace noise while at it.
6 years ago
jsteube 8008d65499 Allow -m 1800 in optimized mode on AMDGPU drivers
6 years ago
jsteube 875718fb8e Backport -m 500 pure kernel code to -m 6300 enables using it on AMDGPU driver
6 years ago
jsteube cd88410781 Backport -m 500 pure kernel code to -m 1600 enables using it on AMDGPU driver
6 years ago
jsteube d7d716f3ab Make it easier to include OpenCL kernels into modules
6 years ago
jsteube 9ced13cc94 Get rid of CONSTSPEC macro in OpenCL kernels
6 years ago
jsteube 13edc32fb4 Fix some unused variable warnings
6 years ago
jsteube 91d9475c11 Plugin refactorization should be finished, no more need for these flags
6 years ago
jsteube 56ecfc3991 No need to risk stability for 400k binary size
6 years ago
jsteube 5951322f72 Testcommit using ar tool in Makefile
6 years ago
Jens Steube cf8c815caf
Merge pull request #1975 from Chick3nman/master
6 years ago
Chick3nman fc1aa83541 Change logic for formatting with multiple devices when some are skipped
6 years ago
Chick3nman 1cf2a4fea6 Fix type missmatch
6 years ago
Chick3nman dc1fc28733 Fix Formatting
6 years ago
Chick3nman 5b20662c7f Fix Formatting
6 years ago
Chick3nman 5e307603d6 Fix formatting
6 years ago
Chick3nman 64f0931301 Switched key name from progress to speed
6 years ago
Chick3nman 3e13739aa6 Fix Typo
6 years ago
Chick3nman 71c02cad5e Add --speed-only and --progress-only support
6 years ago
Chick3nman c2c656edbe Fix missing line
6 years ago
Chick3nman e696e0a87d Fix time formatting
6 years ago
Chick3nman b551592082 Add start and estimated end times, fix formatting
6 years ago
jsteube d855ddaf9e Make use of need_hexify to decide if hexification is needed for ESSID in -m 16800 and -m 16801
6 years ago
jsteube a9663cdb53 For modes 2500, 2501, 16800 and 16801, if --left is used, return original input format
6 years ago
Chick3nman 7bbf4eb183 Fixed restore point number formatting
6 years ago
Chick3nman 4d60c7514a Fixed formatting for speed and progress
6 years ago
Chick3nman ea141f43da Formatting for json status
6 years ago
jsteube e5322c8bee Fix --remove handling in -m 16800 and -m 16801 with new outfile format
6 years ago
jsteube b8d609ba16 WPA/WPA2 cracking: In the potfile, replace password with PMK in order to detect already cracked networks across all WPA modes
6 years ago
jsteube c0a31b3239 Prepare potfile specific module_hash_decode and module_hash_encode hooks
6 years ago
Jens Steube 4115e6b825 Update some unstable_warning on Intel CPU
6 years ago
jsteube 319bf80178 Fix hash_encode() salt position
6 years ago
jsteube 76bf5173ba Do not use MAYBE_UNUSED in inc_common.cl
6 years ago
jsteube 1c45de4b63 Remove more old GCC diagnostic options
6 years ago
jsteube d3a3f10fcf Remove some old GCC diagnostic options
6 years ago
jsteube 708a86fb59 Move old ascii_digest() to hashes.c and rename it to hash_encode(), also remove some unused includes
6 years ago
jsteube f9110c6863 Fix calculation of brute forced PIM
6 years ago
jsteube 9d774958b7 Merge branch 'master' of https://github.com/hashcat/hashcat
6 years ago
jsteube 2158fd70c9 Fix use of OPTS_TYPE_COPY_TMPS in modules
6 years ago
jsteube d80603648e Replace plain_t with void in module_build_plain_postprocess() enables some options
6 years ago
jsteube a7a70c88ed Mark -m 7900 as unstable on ROCM
6 years ago
jsteube 474138f4b9 No more segfaults for -m 12200 with AMDGPU driver
6 years ago
jsteube 792d61763b No more segfaults for -m 8900 and 9300 with AMDGPU driver
6 years ago
jsteube ffd8ec9001 Fixed output password of 'e' rule in pure and cpu rule engine if separator character is also the first letter
6 years ago
jsteube 9d6d2cb2b8 Replace md5_complete_no_limit() code with functions from emu_inc_hash_md5.h
6 years ago
Chick3nman 0cc365139b Added sanity check to confirm --machine-readable and --status-json do not run at the same time.
6 years ago
Chick3nman cac6522cd7 More prep
6 years ago
jsteube 7806be32c2 Add module_unstable_warning() for several modes used with AMDGPU drivers
6 years ago
Chick3nman 81bc4b9ee9 Fixed Typo
6 years ago
Chick3nman 2358220cbe Prepare for --status_json
6 years ago
Jens Steube 06dc04bf1a Use kern_type instead of hash_mode to calculate device_name_chksum
6 years ago
Jens Steube e74e8f0234 Fix device_name_chksum calculation
6 years ago
Jens Steube 0fb3b3c83e Declare internal functions in OpenCL kernels as static
6 years ago
jsteube 69587c91dd Do not use uint if not needed
6 years ago
jsteube 2bb594b385 Remove add3() from bitops, replaced with the ones in inc_common.cl
6 years ago
jsteube ecbd4a51c8 Add remaining emu_inc_* sources to Makefile
6 years ago
jsteube 5b667d2c01 Get rid of src/cpu_aes.c, src/cpu_des.c, src/cpu_md5.c and src/cpu_sha256.c
6 years ago
jsteube fb8a9d7c40 Get rid of cpu_sha1.c
6 years ago
Sein Coray 21a214e26a
Merge branch 'master' of https://github.com/hashcat/hashcat
6 years ago
jsteube 66d94b06e4 Get rid of src/rp_kernel_on_cpu.c and src/rp_kernel_on_cpu_optimized.c and use OpenCL emulated kernel version
6 years ago
Sein Coray 959852a1aa
Merge branch 'master' of https://github.com/hashcat/hashcat
6 years ago
jsteube a44bed7549 More preparation for OpenCL emulation mode
6 years ago
jsteube 0a6fc35707 Fix includes in Makefile
6 years ago
Sein Coray 3ad7d00380
removed hash constants include
6 years ago
jsteube c9d60c079f Prepare OpenCL kernels for non-static compilation
6 years ago
jsteube 7d4bea41a0 Get rid of OpenCL/inc_hash_constants.h and OpenCL/inc_hash_functions.cl
6 years ago
Sein Coray 2da33ab0ba
fixed issue with converting more than needed and using too much memory
6 years ago
Sein Coray 97249ba1ca
added pkzip kernels 17200, 17210, 17220 and 17230
6 years ago
jsteube aec49509b8 Make sure -T does not come in inflict with FIXED_LOCAL_SIZE
6 years ago
jsteube f08fe1fe90 Use advanced memory allocation only on NV and AMD
6 years ago
Jens Steube af129d32da
Merge pull request #1941 from s3inlc/master
6 years ago
Sein Coray 836c91c8c2
Merge branch 'master' of https://github.com/s3inlc/hashcat
6 years ago
Sein Coray 17083b8f56
applied requested final changes
6 years ago
jsteube 5ef67a8ab7 Apply previous blowfish optimization for -m 3200 also on -m 9000 and -m 18600
6 years ago
jsteube a172ab7d8a Update unstable warnings for latest AMDGPU driver
6 years ago
Sein Coray 1143cef606
Merge branch 'master' into master
6 years ago
jsteube ba56f41d26 Abort session if module_hash_binary_count () returns zero
6 years ago
jsteube 5ecbcde945 Cracking bcrypt: Use a feedback from the OpenCL runtime to dynamically find out optimal thread count
6 years ago
jsteube 42e440611a Fix some broken strict-aliasing rules
6 years ago
jsteube b48056fa42 Manually unrolled cipher code fixed segmentation faults in 1536 bit variants for TC/VC with amdgpu-pro-18.50-708488-ubuntu-18.04
6 years ago
jsteube df1ba3745a Mark -m 18600 unstable on POCL runtime
6 years ago
jsteube e93590c11d Fix some variable names in modules
6 years ago
jsteube 218322f630 Support for inline VeraCrypt PIM Brute-Force
6 years ago
Royce Williams 2a739a86ae rewrap --keep-guessing language for console width
6 years ago
jsteube e45e15465b Fix use of OPTS_TYPE_SUGGEST_KG
6 years ago
jsteube b7f8b2d15e Fix use of OPTS_TYPE_SUGGEST_KG
6 years ago
Jens Steube c99ab74001
Merge pull request #1955 from Fist0urs/krb5tgs_1718
6 years ago
jsteube 111889d3fc Keep Guessing: No longer automatically activate --keep-guessing for modes 9720, 9820, 14900 and 18100
6 years ago
Jens Steube 25a9cb58df
Merge pull request #1954 from Fist0urs/krb5tgs
6 years ago
Jens Steube 5e6f5c31de
Merge pull request #1952 from Chick3nman/master
6 years ago
Fist0urs afb010870a Add hash modes 19600 (krb5tgs enctype 17) and 19700 (krb5tgs enctype 18)
6 years ago
Fist0urs 6022443842 m 13100: remove invalid 'pwdump' input format within module
6 years ago
Fist0urs 1cc814bb42 m 13100: append algorithm to hash format name
6 years ago
Chick3nman 3c7d42079e
Update catch for --keep-guessing to include auto-enabled kernels
6 years ago
jsteube 4653447dfa Update startup message with informations on using pure OpenCL kernel
6 years ago
Chick3nman e8b81657d7
Add warning message for --keep-guessing
6 years ago
Chick3nman c0b3f03605
Do not remove hashes if --keep-guessing enabled
6 years ago
jsteube 6e0ef6984c Fix -m 14800 benchmark iteration count
6 years ago
jsteube 756ec0288e Some module specific trap 6 markers
6 years ago
jsteube 2809c6f3fb Some module specific trap 6 markers
6 years ago
jsteube 555bd84b4c Some module specific trap 6 markers
6 years ago
jsteube 26d7602bbd No longer need reqd_work_group_size() in OpenCL kernels since modules taken care of this using threads_min and threads_max
6 years ago
jsteube 9da14d55a2 Some module specific trap 6 markers
6 years ago
jsteube b99d392e78 OpenCL Runtime: Disable OpenCL kernel cache on Apple for Intel CPU (throws CL_BUILD_PROGRAM_FAILURE for no reason)
6 years ago
philsmd 30fde2f759
-m 16600: currently only electrum1 and electrum2 are supported
6 years ago
Jens Steube b585f25c8c Move more no unrolling exceptions from inc_vendor.cl to specific modules
6 years ago
Jens Steube 38cd3f18ee Mark -m 8200 as unstable on Apple OpenCL runtime
6 years ago
Jens Steube 8d146f3011 Move more no unrolling exceptions from inc_vendor.cl to specific modules
6 years ago
Jens Steube cace799187 Move more no unrolling exceptions from inc_vendor.cl to specific modules
6 years ago
Sein Coray ee97d18af9
Added hash mode 19500
6 years ago
jsteube ac0559f7a4 Change the unstable_warning message to the user to make clear it's not a hashcat issue
6 years ago
jsteube 16f8c5941e Mark -m 6100,7500,8600,11700,11800,13100,18200 as unstable with AMDGPU driver in pure kernel mode
6 years ago
jsteube 4d2a0a7738 Mark -m 14400 as unstable with AMDGPU driver
6 years ago
jsteube 745baf4894 Mark -m 11750,11760,11850 and 11860 as unstable with AMDGPU driver
6 years ago
jsteube 277db2ecee Mark VeraCrypt 1536 bit variants as unstable on AMDGPU driver
6 years ago
jsteube 73d4ca14f1 Mark -m 10700 in optimized mode as unstable on Intel OpenCL runtime
6 years ago
jsteube 24f80e1ef4 Mark -m 11600 as unstable with AMDGPU driver
6 years ago
jsteube d325413b34 Fix -m 10700 activate unstable warning only in optimized mode
6 years ago
jsteube 460153d818 Fix -m 6211,6221,6232,6233 module_unstable_warning settings
6 years ago
jsteube 0f8083a8f5 Mark -m 10100 as unstable with ROCM driver
6 years ago
jsteube df38814d25 Mark -m 13731,13732,13733 as unstable with Intel OpenCL runtime. Note this happens only with the 18.x version. The preivous 16.x version compiles this just fine.
6 years ago
jsteube 98eb9ddf6b Fix registration of module_unstable_warning on -m 8900
6 years ago
jsteube 10f5784f7f Mark -m 6231,6232,6233 as unstable with Intel OpenCL runtime. Note this happens only with the 18.x version. The preivous 16.x version compiles this just fine.
6 years ago
jsteube e7e16d00af Fix memory buffer double free
6 years ago
jsteube 1537fc4e5d Improve handling of temporary skipped devices (due to JiT build failure or unstable_warning)
6 years ago
jsteube c43ef406a9 Make sure not to abort entire benchmark if a mode was marked as unstable
6 years ago
jsteube dc9279c95c New Strategy: Instead of using volatile, mark the mode as unstable. Remove all volatiles
6 years ago
jsteube 26b9e3c1ac Fix module_kernel_threads_min and module_kernel_threads_max configuration in -m 9000 module
6 years ago
jsteube b2fb1704ff Fix switched 64 bit optimization in DPAPI masterkey file v1/v2
6 years ago