Will Crozier
edf7365cda
stdout mode: transfer indexes and compressed pw buffer from device in blocks, reducing overhead
2022-02-25 16:35:55 +00:00
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