1
0
mirror of https://github.com/hashcat/hashcat.git synced 2024-11-26 01:50:10 +00:00
Commit Graph

1501 Commits

Author SHA1 Message Date
Jens Steube
6dc45eacc6
Merge pull request #3184 from matrix/metal_opencl_gpu_utilization
Hardware Monitor: Add support for GPU device utilization readings using iokit on Apple Silicon (OpenCL and Metal)
2022-02-18 12:13:52 +01:00
Jens Steube
c7564f0b26
Update types.h
Please use u32 whenever you want to use "uint" or "unsigned int"
2022-02-17 09:48:52 +01:00
Gabriele Gristina
578c7e91d4 fix crossBuild error (windows) 2022-02-17 09:28:29 +01:00
Gabriele Gristina
7eb66e9936 Hardware Monitor: Add support for GPU device utilization readings using iokit on Apple Silicon (OpenCL and Metal) 2022-02-15 22:20:03 +01:00
Chick3nman
16096c8db9 Fix hashcat_status struct 2022-02-14 16:59:14 -06:00
Chick3nman
808e6fff2b Prepare "Net New" value for status, test initial status message format 2022-02-14 16:54:36 -06:00
Gabriele Gristina
3064c63c71 User Options: Change --backend-info/-I option type, from bool to int 2022-02-13 12:33:11 +01:00
Gabriele Gristina
490702fcfa Backends: added Metal host-code 2022-02-05 22:48:16 +01:00
Gabriele Gristina
3ce57b5d2a Added generic system info to backend_info() 2022-01-29 08:15:28 +01:00
Gabriele Gristina
f13948d14c Merge remote-tracking branch 'origin/master' into updated_moduleUnstableWarnings_and_statusCodes 2022-01-24 07:32:41 +01:00
Gabriele Gristina
a1ced24564 Fixed bug on benchmark engine, add some unstable warnings, updated negative status code 2022-01-22 12:10:09 +01:00
Gabriele Gristina
6175459b0a
Merge branch 'hashcat:master' into autotune_error_handling 2022-01-21 20:26:10 +01:00
Jens Steube
aff608fe29
Merge branch 'master' into fix_benchmarkEngine_plus_updated_statusCode 2022-01-15 14:10:59 +01:00
Jens Steube
ee2d50d341
Merge pull request #3117 from DeforaNetworks/khorben/netbsd
Fix the build for NetBSD
2022-01-11 18:49:08 +01:00
Gabriele Gristina
7650894e02 fixed bug in benchmark engine, updated negative status code 2022-01-11 04:58:30 +01:00
Pierre Pronchery
1cb24b0a3c Fix the build for NetBSD 2022-01-10 00:14:45 +01:00
Gabriele Gristina
607d314ff2
Merge branch 'master' into autotune_error_handling 2022-01-07 12:24:39 +01:00
Jens Steube
56ef2b4bde
Merge pull request #3102 from matrix/backend_cuda_restyle
CUDA Backend: moved functions to ext_cuda.c/ext_nvrtc.c and includes to ext_cuda.h/ext_nvrtc.h
2022-01-06 11:29:56 +01:00
Jens Steube
3b49d301db
Merge pull request #3092 from neheb/minizip
remove ioapi include
2022-01-06 10:50:16 +01:00
Jens Steube
668d2179cd Kernels: Refactored standard kernel declaration to use a structure holding u32/u64 attributes to reduce the number of attributes 2022-01-04 18:07:18 +01:00
Gabriele Gristina
3802adff7e Autotune: Added error handling. By default skipping device on error, with --force using accel/loops/threads min values instead 2022-01-04 01:14:39 +01:00
Gabriele Gristina
f8ceb8785e CUDA Backend: moved functions to ext_cuda.c/ext_nvrtc.c and includes to ext_cuda.h/ext_nvrtc.h 2022-01-03 16:29:15 +01:00
Jens Steube
2344cb0365
Merge pull request #3101 from matrix/beautify_ext_OpenCL
beautify ext_OpenCL.h
2022-01-03 09:50:10 +01:00
Gabriele Gristina
4604b53763 beautify ext_OpenCL.h 2022-01-03 02:41:12 +01:00
Gabriele Gristina
78c7ee2af6 HIP Backend: moved functions to ext_hip.c/ext_hiprtc.c and includes to ext_hip.h/ext_hiprtc.h 2022-01-02 19:12:41 +01:00
Rosen Penev
0848484f6f remove ioapi include
ioapi is not available with minizip-ng, which gets used when
USE_SYSTEM_ZLIB is defined.

Signed-off-by: Rosen Penev <rosenp@gmail.com>
2021-12-29 18:17:01 -08:00
Gabriele Gristina
26b6054cab OpenCL Backend: moved functions to ext_OpenCL.c and includes to ext_OpenCL.h 2021-12-28 21:55:05 +01:00
Gabriele Gristina
861e644057 OpenCL Backend: added workaround to make optimized kernels work on Apple Silicon 2021-12-24 17:30:49 +01:00
Jens Steube
5015bc0d2e Module Parser: Renamed struct token_t to hc_token_t to avoid naming conflict with token_t on MacOS 2021-12-20 13:19:40 +01:00
Jens Steube
5b4ac09e91 User Options: Add new module function module_hash_decode_postprocess() to override hash specific configurations from command line 2021-11-28 13:58:27 +01:00
Jens Steube
5389adff81 Usage Screen: On windows console, wait for any keypress if usage_mini_print() is used 2021-11-26 09:53:42 +01:00
Jens Steube
21f91c5bb8 Module Optimizaters: Added OPTS_TYPE_MAXIMUM_THREADS to deactivate the else branch route in the section to find -T before compilation
Set the new flag based on some testings with RX6900XT
2021-11-13 17:27:06 +01:00
Jens Steube
53f6693495 Temporary enable HIP 4.4/ROCM 4.5 on Linux and globally set native thread count 2021-11-10 19:32:54 +01:00
Jens Steube
ae8e52f127 Device Threads: Set back default maximum device thread number to 1024 2021-11-06 20:18:01 +01:00
Jens Steube
d3ae131128 Device Threads: The default maximum device thread number has been reduced from 1024 to 64, users can still overwrite with the -T option 2021-11-04 19:29:34 +01:00
Jens Steube
b768f96228 Device Threads: The default maximum device thread number has been reduced from 1024 to 256, users can still overwrite with the -T option 2021-11-03 09:08:17 +01:00
Jukka Ojanen
3cacbe0e1f Add support for xz compressed files 2021-08-25 16:56:55 +03:00
Jukka Ojanen
3bc7b6af90 Avoid directly accessing file handle 2021-08-21 14:29:10 +03:00
Jens Steube
50e28ff306
Merge pull request #2926 from jtojanen/master
Code cleanup and small fixes
2021-08-19 14:59:16 +02:00
Jukka Ojanen
fed32a58c7 Always cleanup and initialize all parts of HC_FILE structure 2021-08-18 19:28:00 +03:00
Jukka Ojanen
f3cd32bffd Avoid memory copy in rebuild_pws_compressed_append() and assign instead 2021-08-18 17:46:39 +03:00
Jens Steube
76e388ea47 Memory Management: Check in OpenCL that CL_DEVICE_HOST_UNIFIED_MEMORY is true and if so, then half of the available memory
NEO driver: Activate the NEO driver (Intel GPU) after it passed several tests in hashcat using the latest NEO driver version
2021-08-18 16:10:51 +02:00
Jens Steube
9254603960 Fixed out-of-boundary read in PKZIP masterkey kernel if the password candidate has length zero.
Now that kernel threads are no longer fixed over the entire session, hardware_power and hardware_power_all
needs to be updated the same way as kernel_power and kernel_power_all for each call to inner2_loop().
2021-08-17 17:38:45 +02:00
Jens Steube
05f107cbe5 Added option --generate-rules-func-sel to specify a pool of operators that the random rule generator is allowed to pick from 2021-08-14 11:43:32 +02:00
Jens Steube
6b485dd3fd
Merge pull request #2934 from jtojanen/fix_extra_tmp_size
Assume hashconfig->tmp_size is the element size
2021-08-14 10:06:55 +02:00
Jukka Ojanen
5c0820b8d3 Assume hashconfig->tmp_size is the element size 2021-08-13 13:13:12 +03:00
Jens Steube
1f22984313 The hc_bytealign_be_S() was merged too early, but is not yet used anywhere for this platform so we can remove it again. 2021-08-12 15:15:32 +02:00
Jens Steube
01738fafa0 Deprecated Plugins: Add new module function module_deprecated_notice() to mark a plugin as deprecated and to return a free text user notice
Added option --deprecated-check-disable to enable deprecated plugins
2021-08-10 17:59:52 +02:00
Jens Steube
63a0c5a1e1
Merge branch 'master' into snmpv3_sha512 2021-08-04 21:05:42 +02:00
Jens Steube
dde75f2763
Merge pull request #2904 from matrix/snmpv3_sha384
Added hash-mode: SNMPv3 HMAC-SHA384-256
2021-08-04 21:04:55 +02:00
Jens Steube
cb69e2d413 Added some HIP version checks, fall back to OpenCL automatically
Switched HIP version check from driverVersion to runtimeVersion
Fixed syntax check of HAS_VPERM macro in several kernel includes causing invalid error message for AMD GPUs on Windows
Updated AMD driver requirements
Updated docs/changes.txt with missing changes from previous commits
Fixed invalid vector data type in Murmur Hash in -a 3 mode
Fixed uninitialized variable warning in src/hashes.c
Fixed broken support for --generate-rules-func-min
2021-08-04 20:49:22 +02:00
Jens Steube
af5d346244
Merge pull request #2894 from jtojanen/master
Allow async execution
2021-08-02 10:05:20 +02:00
Jens Steube
20a7b9f992 Tuning-Database: Add new module function module_extra_tuningdb_block() to extend hashcat.hctune content from a plugin
See src/modules/module_08900.c as an example
2021-08-01 16:25:37 +02:00
Jukka Ojanen
3d7ce7162b Merge branch 'master' of https://github.com/hashcat/hashcat 2021-08-01 15:36:52 +03:00
Jens Steube
f4e52ca533 Add new rule function '3' to switch the case of the first letter after occurrence N of char X 2021-08-01 00:04:10 +02:00
Jukka Ojanen
c3195d0603 Merge branch 'master' of https://github.com/hashcat/hashcat 2021-07-30 11:34:25 +03:00
Jukka Ojanen
d7cc8d7cd2 Revert due to module_03200.c, module_25600.c and module_25800.c using device_param->kernel_dynamic_local_mem_size_memset 2021-07-28 19:49:02 +03:00
Jukka Ojanen
8b590f651b Remove unused gpu_memset and its references 2021-07-28 19:26:30 +03:00
Jens Steube
ae39fa0979
Merge pull request #2908 from hashcat/master
Backports
2021-07-28 07:55:11 +02:00
Jukka Ojanen
5dbe4958b8 Remove digests_shown_tmp buffer, used in check_cracked() to zero out hashes 2021-07-27 19:01:13 +03:00
Jukka Ojanen
cdf27a1cb3 Implement async run_cuda_kernel_memset() and run_cuda_kernel_memset32() 2021-07-27 18:56:59 +03:00
Jukka Ojanen
be33ccaa6c check_hash() needs to return value to indicate possible error 2021-07-27 14:36:48 +03:00
Jens Steube
532a154542 ADL: Updated support for AMD Display Library to 15.0, updated datatypes and added support for OverDrive 7 and 8 based GPUs 2021-07-27 12:02:27 +02:00
Jukka Ojanen
d7de3550b1 Add fast event for CUDA and HIP, and use it to synchronize check_hash() 2021-07-27 12:57:26 +03:00
Gabriele Gristina
357c23d7a1 Added hash-mode: SNMPv3 HMAC-SHA384-256 2021-07-27 05:17:26 +02:00
Gabriele Gristina
15b90c953e Added hash-mode: SNMPv3 HMAC-SHA512-384 2021-07-27 05:14:09 +02:00
Jukka Ojanen
a642f7b233 Remove synchronous GPU memory copy functions 2021-07-26 15:36:42 +03:00
Jens Steube
b66c093c17
Merge pull request #2902 from hashcat/master
Backports
2021-07-26 08:18:35 +02:00
Jens Steube
b53691c8f5 ADL: Updated support for AMD Display Library to 14.0, updated datatypes and added support for OverDrive 7 and 8 based GPUs 2021-07-26 07:48:56 +02:00
Jukka Ojanen
4bd7363674 Add missing HIP declarations 2021-07-25 22:18:16 +03:00
Jens Steube
72e307fbce
Merge pull request #2901 from hashcat/master
Backport changes
2021-07-25 10:57:39 +02:00
Jens Steube
959a232828
Merge pull request #2885 from neheb/charfixes
const and char fixes
2021-07-25 10:36:40 +02:00
Jens Steube
84a4058edf
Merge pull request #2900 from hashcat/master
Backport changes
2021-07-25 10:34:05 +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
Jens Steube
5ffcaa980d HIP Backend: Added support to support HIP 4.4 and later, but added check to rule out older versions because they are incompatible 2021-07-23 16:04:34 +02:00
Rosen Penev
14f5a26027 use const char for fopen mode
Fixes -Wwrite-strings warnings.

Signed-off-by: Rosen Penev <rosenp@gmail.com>
2021-07-22 18:11:11 -07: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
Jukka Ojanen
fafd24237d Define HC_ALIGN macro to control data alignment and use common constant zero buffer in run_cuda_kernel_bzero(), run_hip_kernel_bzero() and run_opencl_kernel_bzero(). 2021-07-22 14:24:03 +03: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
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
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
ea5180ac46 Include missing bzero kernel parameters 2021-07-20 11:59:44 +03:00
Jukka Ojanen
a2a1d04bcf Implement gpu_bzero 2021-07-17 19:00:10 +03:00
Jens Steube
1ab56afb9e
Merge pull request #2874 from hashcat/master
Backports from master
2021-07-12 08:57:50 +02:00
Jens Steube
ca3beacd93 Disable dynamic shared memory on HIP, because hipFuncSetAttribute() maps to cudaFuncSetAttribute() and not to cuFuncSetAttribute() 2021-07-11 14:30:49 +02:00
Jens Steube
92cf955ae6
Merge pull request #2872 from jtojanen/master
Use critical section instead of mutex in Windows
2021-07-11 13:43:11 +02:00
Jens Steube
1b84a9e53b Add missing backports from code base v6.2.2
Fix context to thread management
Fix missing code in selftest.c, autotune.c, hashes.c, dispatch.c and backend.c
Use IS_HIP depending code makes it easier for future optimization related to inline assembly calls - instead of using IS_CUDA || IS_HIP
See TODO markers for more optimizations / next steps
2021-07-11 12:38:59 +02:00
Jens Steube
a22f8149fc
Merge branch 'HIP' into hip 2021-07-10 21:34:09 +02:00
Jukka Ojanen
2fd0a81f93 Use critical section instead of mutex in Windows 2021-07-10 16:29:40 +03:00
Jens Steube
9fc6c26f8c Added temperature watchdog and utilization for CPU on linux using sysfs and procfs 2021-07-10 14:24:51 +02:00
Jens Steube
bfe83ec138 Added temperature watchdog for CPU on linux using sysfs 2021-07-10 08:43:15 +02:00
Jens Steube
979f9e9868 Rename hardware monitor interface sysfs to sysfs_amdgpu 2021-07-09 20:48:10 +02:00
reger-men
ea7b74389f First draft HIP Version 2021-07-09 03:50:40 +00:00
Jens Steube
f146a05878 Added option --markov-inverse to inverse markov statistics, with the idea of reversing the order of the password candidates 2021-07-07 10:32:08 +02:00
Jens Steube
701ad7c441 Fix segfault in --hash-info by avoid huge stack buffer allocation 2021-06-30 21:01:55 +02:00
Jens Steube
56c2243dfb KeePass: Increase supported size for KeePass 1 databases from 300kB to 16MB 2021-06-30 13:16:03 +02:00
Jens Steube
254e33c473 File handling: Do not abort on seeing a BOM in input files, just warn and ignore the BOM 2021-06-29 20:42:22 +02:00
Jens Steube
2af45cd03f Rename hc_fopen_nozip() to hc_fopen_raw() 2021-06-29 20:13:11 +02:00
Jens Steube
dcaba1f473 Brain: Add brain_ctx_t to hashcat_ctx_t to enable runtime check if hashcat was compiled with brain support 2021-06-26 20:24:45 +02:00