Commit Graph

3981 Commits

Author SHA1 Message Date
Gabriele Gristina
87f7bc59e3 reduced the amount of memory allocated in gpu for SNMPv3 HMAC-SHA384-256 2021-08-03 21:29:07 +02:00
Gabriele Gristina
357c23d7a1 Added hash-mode: SNMPv3 HMAC-SHA384-256 2021-07-27 05:17:26 +02:00
Jens Steube
640d95a00f Vendor Detection: Add "Intel" as a valid vendor name for GPU on macOS 2021-07-24 16:01:30 +02:00
Gabriele Gristina
4f10377703 Added hash-mode: SNMPv3 HMAC-MD5-96 2021-07-24 13:56:49 +02:00
Jens Steube
3a31b669b5 Optimize and clean up -m 25200 code.
Speed on CPU: 1521 -> 2066 (35% faster)
Speed on GPU: 16610 -> 157754 (9.4 times faster)
Works for all password lengths
2021-07-24 11:58:36 +02:00
Jens Steube
5e0f7ecf00 Merge pull request #2889 from matrix/snmpv3_sha1
Added hash-mode: SNMPv3 HMAC-SHA1-96
2021-07-24 11:56:46 +02:00
Gabriele Gristina
4fb44f826c updated module_25200.c as requested in the review 2021-07-24 10:57:06 +02:00
Gabriele Gristina
b00e3e5e59 add missing hex_encode() in module_hash_encode() 2021-07-22 19:53:41 +02:00
Gabriele Gristina
6d83a69f7d using hex_encode/hex_decode + small fixes 2021-07-22 19:10:34 +02:00
Jens Steube
f9e74045b5 Commandline: Throw an error if separator character given by the user with -p option is not exactly 1 byte 2021-07-22 18:54:02 +02:00
Jens Steube
5024865d87 Kernel Threads: Use warp size / wavefront size query instead of hardcoded values as base for kernel threads
Kernel Cache: Add kernel threads into hash computation which is later used in the kernel cache filename
Remove some unused function symbol lookups in HIP library
2021-07-22 11:46:47 +02:00
Jens Steube
e83611742d Brain Session: Adds hashconfig specific opti_type and opts_type parameters to hashcat session computation to cover features like -O and -M 2021-07-21 15:47:26 +02:00
Jens Steube
c990e252d3 Added option --multiply-accel-disable (short: -M) to disable multiply the kernel-accel with the multiprocessor count automatism 2021-07-21 15:47:05 +02:00
Jens Steube
a7a899e5a4 Backport changes from #2888 to HIP backend 2021-07-21 14:01:28 +02:00
Jukka Ojanen
cb923d6e46 Replace CU_DEVICE_ATTRIBUTE_MAX_SHARED_MEMORY_PER_BLOCK with CU_DEVICE_ATTRIBUTE_MAX_SHARED_MEMORY_PER_BLOCK_OPTIN 2021-07-21 13:42:22 +03:00
Gabriele Gristina
7ea5da51a8 Added hash-mode: SNMPv3 HMAC-SHA1-96 2021-07-20 22:24:35 +02:00
Jukka Ojanen
55a475cb4b Merge branch 'hashcat:master' into master 2021-07-20 21:27:51 +03:00
Jukka Ojanen
d23f2d6c2f Calculation kernel dynamic memory size based on CU_DEVICE_ATTRIBUTE_MAX_SHARED_MEMORY_PER_BLOCK 2021-07-20 21:27:29 +03:00
Jens Steube
a026171fb3 Merge pull request #2879 from jtojanen/master
Implement gpu_bzero
2021-07-20 13:00:37 +02:00
Jens Steube
7c5fe5e233 Slow Kernels: Set some of the slowest kernels to OPTS_TYPE_MP_MULTI_DISABLE 2021-07-20 12:47:40 +02:00
Jukka Ojanen
8674e23d79 Add async HIP memcpy functions: hc_hipMemcpyDtoDAsync(), hc_hipMemcpyDtoHAsync() and hc_hipMemcpyHtoDAsync(). Implement partially async HIP memset and bzero kernels. 2021-07-20 12:47:10 +03:00
Jukka Ojanen
4263cafdcf Add async CUDA memcpy functions: hc_cuMemcpyDtoDAsync(), hc_cuMemcpyDtoHAsync() and hc_cuMemcpyHtoDAsync(). Implement partially async CUDA memset and bzero kernels. 2021-07-20 12:23:39 +03:00
Jukka Ojanen
f07ff6f03d Use kernel_bzero instead of kernel_memset when value is zero 2021-07-20 12:04:12 +03:00
Jukka Ojanen
4c0f6dd263 Merge branch 'hashcat:master' into master 2021-07-20 12:00:41 +03:00
Jukka Ojanen
ea5180ac46 Include missing bzero kernel parameters 2021-07-20 11:59:44 +03:00
Jens Steube
7d43b6e1eb Clear tmps memory region after autotune use 2021-07-19 11:59:53 +02:00
Jens Steube
0504498e86 Merge pull request #2886 from pellekuiters/issue-2876
Auto-tuning outside kernel can cause unpredictable behavior for tmp_t structs on CUDA
2021-07-19 11:52:07 +02:00
pelle
ac3ccfcc51 Run init() and loop_prepare() during autotune to prevent possible corruptions during loop(). 2021-07-19 11:07:24 +02:00
Jens Steube
257098a301 Get rid of hip/hip_runtime.h dependancy 2021-07-18 21:14:45 +02:00
Jukka Ojanen
72a418932c HIP: Use kernel_bzero instead of kernel_memset when value is zero 2021-07-17 19:12:09 +03:00
Jukka Ojanen
a2a1d04bcf Implement gpu_bzero 2021-07-17 19:00:10 +03:00
Jukka Ojanen
8066a47ac5 Merge branch 'hashcat:master' into master 2021-07-17 16:21:08 +03:00
Jens Steube
261e0f42ab Unset PRODUCTION option 2021-07-16 23:03:11 +02:00
Jens Steube
84082a952e hashcat 6.2.3 2021-07-16 22:41:52 +02:00
Jens Steube
141b59b80e Merge pull request #2883 from hashcat/HIP
Merge HIP branch into master
2021-07-16 19:54:00 +02:00
Jens Steube
45e65dd05a Backport more ROCm based optimizations to HIP 2021-07-15 23:34:27 +02:00
Jens Steube
2e929e692e Backport update module_unstable_warning() for -m 21800 on HIP 2021-07-15 21:26:07 +02:00
Jens Steube
4730cf6e79 WinZip Kernel: Increase supported data length from 8k to 16mb 2021-07-15 16:42:29 +02:00
Jens Steube
d130cc66b3 Optimize ISA code on HIP for V_ALIGNBIT_B32 using a different template for inline assembly 2021-07-15 09:57:41 +02:00
Gabriele Gristina
80a671eab7 Fix bug on hm_SYSFS_CPU_get_syspath_hwmon() 2021-07-14 19:21:21 +02:00
Jens Steube
cf512faa53 Update large switch() cases in inc_common.cl and some inline assembly common functions for devices managed with HIP backend 2021-07-14 17:06:20 +02:00
Jens Steube
11295e4679 Fix missing OPTI_TYPE_USES_BITS_64 in several modules 2021-07-14 17:01:46 +02:00
Jukka Ojanen
43b5a138d4 Use kernel_bzero instead of kernel_memset when value is zero 2021-07-14 17:13:39 +03:00
Jens Steube
a82fce2c8f Fixed invalid ETA if --limit was specified, several salts are in a hash list and some of them were found in a potfile 2021-07-14 10:26:57 +02:00
Jens Steube
9c134833a6 Update module_unstable_warning() for -m 19600 and -m 19700 2021-07-14 08:26:12 +02:00
Jens Steube
f3bd936971 Add hardware monitor mapping for HIP devices 2021-07-14 08:23:39 +02:00
Jens Steube
84fcea9592 Fix unusued variable warning 2021-07-14 08:17:55 +02:00
Jens Steube
4b68a8fb4f Merge pull request #2878 from hashcat/master
Backports
2021-07-13 22:26:28 +02:00
Jens Steube
7faf6859d6 Backport hand-optimized compiler settings in modules from ROCM to HIP
Backport DECLSPEC settings from ROCM to HIP
2021-07-13 20:45:01 +02:00
Jens Steube
74fca7bac1 Merge pull request #2875 from jtojanen/master
Fix leaks in dictstat_destroy
2021-07-13 13:28:37 +02:00