Will Crozier
edf7365cda
stdout mode: transfer indexes and compressed pw buffer from device in blocks, reducing overhead
3 years ago
Gabriele Gristina
490702fcfa
Backends: added Metal host-code
3 years ago
Gabriele Gristina
f8ceb8785e
CUDA Backend: moved functions to ext_cuda.c/ext_nvrtc.c and includes to ext_cuda.h/ext_nvrtc.h
3 years ago
Gabriele Gristina
78c7ee2af6
HIP Backend: moved functions to ext_hip.c/ext_hiprtc.c and includes to ext_hip.h/ext_hiprtc.h
3 years ago
Gabriele Gristina
26b6054cab
OpenCL Backend: moved functions to ext_OpenCL.c and includes to ext_OpenCL.h
3 years ago
Jukka Ojanen
f3cd32bffd
Avoid memory copy in rebuild_pws_compressed_append() and assign instead
3 years ago
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
3 years ago
Jukka Ojanen
c3195d0603
Merge branch 'master' of https://github.com/hashcat/hashcat
3 years ago
Jukka Ojanen
cdf27a1cb3
Implement async run_cuda_kernel_memset() and run_cuda_kernel_memset32()
3 years ago
Jukka Ojanen
a642f7b233
Remove synchronous GPU memory copy functions
3 years ago
Jukka Ojanen
4bd7363674
Add missing HIP declarations
3 years ago
Jens Steube
84a4058edf
Merge pull request #2900 from hashcat/master
...
Backport changes
3 years ago
Jens Steube
640d95a00f
Vendor Detection: Add "Intel" as a valid vendor name for GPU on macOS
3 years ago
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
3 years ago
Jukka Ojanen
4263cafdcf
Add async CUDA memcpy functions: hc_cuMemcpyDtoDAsync(), hc_cuMemcpyDtoHAsync() and hc_cuMemcpyHtoDAsync(). Implement partially async CUDA memset and bzero kernels.
3 years ago
Jens Steube
ca3beacd93
Disable dynamic shared memory on HIP, because hipFuncSetAttribute() maps to cudaFuncSetAttribute() and not to cuFuncSetAttribute()
3 years ago
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
3 years ago
Jens Steube
a22f8149fc
Merge branch 'HIP' into hip
3 years ago
reger-men
ea7b74389f
First draft HIP Version
3 years ago
nycex
470e844e5d
use XDG_CACHE_HOME for kernels
3 years ago
Jens Steube
5c6501444a
Kernels: Add standalone true UTF8 to UTF16 converter kernel that runs after amplifier. Use OPTS_TYPE_POST_AMP_UTF16LE from plugin
3 years ago
Jens Steube
0c2afde83b
Add support for clUnloadPlatformCompiler()
3 years ago
Jens Steube
a0eae9050c
OpenCL Runtime: Workaround JiT compiler deadlock on NVIDIA driver >= 465.89
4 years ago
Jens Steube
04d5e5a119
New Attack-Mode: Association Attack. Like JtR's single mode. Very early
...
stage. See hashcat Forum for detailed writeup.
4 years ago
Jens Steube
1fc37c25f9
OpenCL Kernels: Moved "gpu_decompress", "gpu_memset" and "gpu_atinit" into new OpenCL/shared.cl in order to reduce compile time
5 years ago
Jens Steube
346637ec43
Improve cujit logging
5 years ago
Jens Steube
66ae5125ce
Cache cubin instead of PTX to decrease startup time
5 years ago
Jens Steube
a8555fa048
Support use of all available CPU cores for hash-mode specific hooks
5 years ago
Rosen Penev
6ecb42b3ea
Run through Clang's readability-inconsistent-declaration-parameter-name
5 years ago
Jens Steube
5e0eb288c9
Use __launch_bounds__ in CUDA as replacement for reqd_work_group_size() in OpenCL
5 years ago
Jens Steube
0568c0746a
Emulate effect of reqd_work_group_size() in CUDA
5 years ago
Jens Steube
44ecc83d82
Do some CUDA and NVRTC version checks on startup
5 years ago
Jens Steube
1f6c82b6d1
Add hc_cuModuleLoadDataExLog wrapper function for more detailed error logging from CUDA
5 years ago
Jens Steube
ce8a6fde0a
Fix status screen current password query
5 years ago
Jens Steube
33028314f0
Add hc_cuCtxSetCacheConfig()
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
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
d73c0ac8a9
More CUDA attribute queries
5 years ago
Jens Steube
a415422123
Initialize CUDA devices and some first attribute queries
5 years ago
Jens Steube
9faba41848
Use nvrtc to compile PTX (resulting PTX not yet used)
6 years ago
Jens Steube
4b986de5fb
Prepare native CUDA hybrid integration
6 years ago