arno/hashcat
1
0
Fork 0
mirror of https://github.com/hashcat/hashcat.git synced 2024-11-23 00:28:11 +00:00
Code Issues Releases Wiki Activity
fe847bd569
hashcat/include/ext_OpenCL.h

123 lines
7.5 KiB
C
Raw Normal View History

Initial commit
2015-12-04 14:47:52 +00:00
/**
Added docs/credits.txt Added docs/team.txt
2016-09-11 20:20:15 +00:00
* Author......: See docs/credits.txt
Initial commit
2015-12-04 14:47:52 +00:00
* License.....: MIT
*/
Replace #pragma once with #ifndef #define #endif logic because #pragma once does not work cleanly on OSX
2016-09-06 16:44:05 +00:00
#ifndef _EXT_OPENCL_H
#define _EXT_OPENCL_H
Initial commit
2015-12-04 14:47:52 +00:00
Add support for latest OpenCL headers from Khronos
2018-10-14 10:39:11 +00:00
#define CL_TARGET_OPENCL_VERSION 120
Move tuningdb specific functions into their own source file
2016-09-06 17:44:27 +00:00
#define CL_USE_DEPRECATED_OPENCL_1_2_APIS
#define CL_USE_DEPRECATED_OPENCL_2_0_APIS
Replace all #ifdef with #if defined (...) for convention
2016-09-07 20:29:57 +00:00
#if defined (__APPLE__)
Move tuningdb specific functions into their own source file
2016-09-06 17:44:27 +00:00
#include <OpenCL/cl.h>
Only Apple has a different cl.h location. Simplify a bit
2017-03-05 02:28:50 +00:00
#else
Fix compilation for native Cygwin
2016-11-29 21:39:22 +00:00
#include <CL/cl.h>
#endif
Query PCI-Express bus/device/function and store for later use
2016-11-05 19:23:05 +00:00
// NVIDIA extras
#define CL_DEVICE_COMPUTE_CAPABILITY_MAJOR_NV 0x4000
#define CL_DEVICE_COMPUTE_CAPABILITY_MINOR_NV 0x4001
#define CL_DEVICE_KERNEL_EXEC_TIMEOUT_NV 0x4005
#define CL_DEVICE_PCI_BUS_ID_NV 0x4008
#define CL_DEVICE_PCI_SLOT_ID_NV 0x4009
// AMD extras
#define CL_DEVICE_TOPOLOGY_AMD 0x4037
typedef union
{
struct { cl_uint type; cl_uint data[5]; } raw;
struct { cl_uint type; cl_char unused[17]; cl_char bus; cl_char device; cl_char function; } pcie;
} cl_device_topology_amd;
Create real cpu_crc32.c and rp_cpu.c
2016-09-06 13:28:56 +00:00
#define CL_PLATFORMS_MAX 16
Preparation for easier integration of: * https://github.com/hashcat/hashcat/pull/485 * https://github.com/hashcat/hashcat/pull/486
2016-09-05 19:47:26 +00:00
Get rid of exit() calls in OpenCL wrapper library with the goal to have a better control which error can be ignored under special circumstances Note, not all return codes from some of the subfunctions are uset yet, it would be too much changes at once This is a preparation for https://github.com/hashcat/hashcat/issues/416
2016-07-10 11:23:06 +00:00
typedef cl_int (CL_API_CALL *OCL_CLBUILDPROGRAM) (cl_program, cl_uint, const cl_device_id *, const char *, void (CL_CALLBACK *)(cl_program, void *), void *);
OpenCL Runtime: Workaround JiT compiler deadlock on NVIDIA driver >= 465.89
2021-04-11 11:35:40 +00:00
typedef cl_int (CL_API_CALL *OCL_CLCOMPILEPROGRAM) (cl_program, cl_uint, const cl_device_id *, const char *, cl_uint, const cl_program *, const char **, void (CL_CALLBACK *)(cl_program, void *), void *);
Get rid of exit() calls in OpenCL wrapper library with the goal to have a better control which error can be ignored under special circumstances Note, not all return codes from some of the subfunctions are uset yet, it would be too much changes at once This is a preparation for https://github.com/hashcat/hashcat/issues/416
2016-07-10 11:23:06 +00:00
typedef cl_mem (CL_API_CALL *OCL_CLCREATEBUFFER) (cl_context, cl_mem_flags, size_t, void *, cl_int *);
typedef cl_command_queue (CL_API_CALL *OCL_CLCREATECOMMANDQUEUE) (cl_context, cl_device_id, cl_command_queue_properties, cl_int *);
typedef cl_context (CL_API_CALL *OCL_CLCREATECONTEXT) (const cl_context_properties *, cl_uint, const cl_device_id *, void (CL_CALLBACK *)(const char *, const void *, size_t, void *), void *, cl_int *);
typedef cl_kernel (CL_API_CALL *OCL_CLCREATEKERNEL) (cl_program, const char *, cl_int *);
typedef cl_program (CL_API_CALL *OCL_CLCREATEPROGRAMWITHBINARY) (cl_context, cl_uint, const cl_device_id *, const size_t *, const unsigned char **, cl_int *, cl_int *);
typedef cl_program (CL_API_CALL *OCL_CLCREATEPROGRAMWITHSOURCE) (cl_context, cl_uint, const char **, const size_t *, cl_int *);
typedef cl_int (CL_API_CALL *OCL_CLENQUEUECOPYBUFFER) (cl_command_queue, cl_mem, cl_mem, size_t, size_t, size_t, cl_uint, const cl_event *, cl_event *);
typedef void * (CL_API_CALL *OCL_CLENQUEUEMAPBUFFER) (cl_command_queue, cl_mem, cl_bool, cl_map_flags, size_t, size_t, cl_uint, const cl_event *, cl_event *, cl_int *);
typedef cl_int (CL_API_CALL *OCL_CLENQUEUENDRANGEKERNEL) (cl_command_queue, cl_kernel, cl_uint, const size_t *, const size_t *, const size_t *, cl_uint, const cl_event *, cl_event *);
typedef cl_int (CL_API_CALL *OCL_CLENQUEUEREADBUFFER) (cl_command_queue, cl_mem, cl_bool, size_t, size_t, const void *, cl_uint, const cl_event *, cl_event *);
typedef cl_int (CL_API_CALL *OCL_CLENQUEUEUNMAPMEMOBJECT) (cl_command_queue, cl_mem, void *, cl_uint, const cl_event *, cl_event *);
typedef cl_int (CL_API_CALL *OCL_CLENQUEUEWRITEBUFFER) (cl_command_queue, cl_mem, cl_bool, size_t, size_t, const void *, cl_uint, const cl_event *, cl_event *);
typedef cl_int (CL_API_CALL *OCL_CLFINISH) (cl_command_queue);
typedef cl_int (CL_API_CALL *OCL_CLFLUSH) (cl_command_queue);
typedef cl_int (CL_API_CALL *OCL_CLGETDEVICEIDS) (cl_platform_id, cl_device_type, cl_uint, cl_device_id *, cl_uint *);
typedef cl_int (CL_API_CALL *OCL_CLGETDEVICEINFO) (cl_device_id, cl_device_info, size_t, void *, size_t *);
typedef cl_int (CL_API_CALL *OCL_CLGETEVENTINFO) (cl_event, cl_event_info, size_t, void *, size_t *);
typedef cl_int (CL_API_CALL *OCL_CLGETEVENTPROFILINGINFO) (cl_event, cl_profiling_info, size_t, void *, size_t *);
typedef cl_int (CL_API_CALL *OCL_CLGETKERNELWORKGROUPINFO) (cl_kernel, cl_device_id, cl_kernel_work_group_info, size_t, void *, size_t *);
typedef cl_int (CL_API_CALL *OCL_CLGETPLATFORMIDS) (cl_uint, cl_platform_id *, cl_uint *);
typedef cl_int (CL_API_CALL *OCL_CLGETPLATFORMINFO) (cl_platform_id, cl_platform_info, size_t, void *, size_t *);
typedef cl_int (CL_API_CALL *OCL_CLGETPROGRAMBUILDINFO) (cl_program, cl_device_id, cl_program_build_info, size_t, void *, size_t *);
typedef cl_int (CL_API_CALL *OCL_CLGETPROGRAMINFO) (cl_program, cl_program_info, size_t, void *, size_t *);
OpenCL Runtime: Workaround JiT compiler deadlock on NVIDIA driver >= 465.89
2021-04-11 11:35:40 +00:00
typedef cl_program (CL_API_CALL *OCL_CLLINKPROGRAM) (cl_context, cl_uint, const cl_device_id *, const char *, cl_uint, const cl_program *, void (CL_CALLBACK *) (cl_program, void *), void *, cl_int *);
Get rid of exit() calls in OpenCL wrapper library with the goal to have a better control which error can be ignored under special circumstances Note, not all return codes from some of the subfunctions are uset yet, it would be too much changes at once This is a preparation for https://github.com/hashcat/hashcat/issues/416
2016-07-10 11:23:06 +00:00
typedef cl_int (CL_API_CALL *OCL_CLRELEASECOMMANDQUEUE) (cl_command_queue);
typedef cl_int (CL_API_CALL *OCL_CLRELEASECONTEXT) (cl_context);
typedef cl_int (CL_API_CALL *OCL_CLRELEASEEVENT) (cl_event);
typedef cl_int (CL_API_CALL *OCL_CLRELEASEKERNEL) (cl_kernel);
typedef cl_int (CL_API_CALL *OCL_CLRELEASEMEMOBJECT) (cl_mem);
typedef cl_int (CL_API_CALL *OCL_CLRELEASEPROGRAM) (cl_program);
typedef cl_int (CL_API_CALL *OCL_CLSETKERNELARG) (cl_kernel, cl_uint, size_t, const void *);
Add support for clUnloadPlatformCompiler()
2021-05-02 08:15:25 +00:00
typedef cl_int (CL_API_CALL *OCL_CLUNLOADPLATFORMCOMPILER) (cl_platform_id);
Get rid of exit() calls in OpenCL wrapper library with the goal to have a better control which error can be ignored under special circumstances Note, not all return codes from some of the subfunctions are uset yet, it would be too much changes at once This is a preparation for https://github.com/hashcat/hashcat/issues/416
2016-07-10 11:23:06 +00:00
typedef cl_int (CL_API_CALL *OCL_CLWAITFOREVENTS) (cl_uint, const cl_event *);
Implemented OpenCL library loader
2016-01-26 20:40:49 +00:00
Give all those anonymous structures a name, makes it easier to load the project into VS
2016-10-01 09:54:00 +00:00
typedef struct hc_opencl_lib
Implemented OpenCL library loader
2016-01-26 20:40:49 +00:00
{
Refresh dynloader management
2019-01-14 09:11:23 +00:00
hc_dynlib_t lib;
Implemented OpenCL library loader
2016-01-26 20:40:49 +00:00
Get rid of exit() calls in OpenCL wrapper library with the goal to have a better control which error can be ignored under special circumstances Note, not all return codes from some of the subfunctions are uset yet, it would be too much changes at once This is a preparation for https://github.com/hashcat/hashcat/issues/416
2016-07-10 11:23:06 +00:00
OCL_CLBUILDPROGRAM clBuildProgram;
OpenCL Runtime: Workaround JiT compiler deadlock on NVIDIA driver >= 465.89
2021-04-11 11:35:40 +00:00
OCL_CLCOMPILEPROGRAM clCompileProgram;
Get rid of exit() calls in OpenCL wrapper library with the goal to have a better control which error can be ignored under special circumstances Note, not all return codes from some of the subfunctions are uset yet, it would be too much changes at once This is a preparation for https://github.com/hashcat/hashcat/issues/416
2016-07-10 11:23:06 +00:00
OCL_CLCREATEBUFFER clCreateBuffer;
OCL_CLCREATECOMMANDQUEUE clCreateCommandQueue;
OCL_CLCREATECONTEXT clCreateContext;
OCL_CLCREATEKERNEL clCreateKernel;
Implemented OpenCL library loader
2016-01-26 20:40:49 +00:00
OCL_CLCREATEPROGRAMWITHBINARY clCreateProgramWithBinary;
OCL_CLCREATEPROGRAMWITHSOURCE clCreateProgramWithSource;
Get rid of exit() calls in OpenCL wrapper library with the goal to have a better control which error can be ignored under special circumstances Note, not all return codes from some of the subfunctions are uset yet, it would be too much changes at once This is a preparation for https://github.com/hashcat/hashcat/issues/416
2016-07-10 11:23:06 +00:00
OCL_CLENQUEUECOPYBUFFER clEnqueueCopyBuffer;
OCL_CLENQUEUEMAPBUFFER clEnqueueMapBuffer;
OCL_CLENQUEUENDRANGEKERNEL clEnqueueNDRangeKernel;
OCL_CLENQUEUEREADBUFFER clEnqueueReadBuffer;
OCL_CLENQUEUEUNMAPMEMOBJECT clEnqueueUnmapMemObject;
OCL_CLENQUEUEWRITEBUFFER clEnqueueWriteBuffer;
OCL_CLFINISH clFinish;
OCL_CLFLUSH clFlush;
OCL_CLGETDEVICEIDS clGetDeviceIDs;
OCL_CLGETDEVICEINFO clGetDeviceInfo;
OCL_CLGETEVENTINFO clGetEventInfo;
OCL_CLGETEVENTPROFILINGINFO clGetEventProfilingInfo;
OCL_CLGETKERNELWORKGROUPINFO clGetKernelWorkGroupInfo;
OCL_CLGETPLATFORMIDS clGetPlatformIDs;
OCL_CLGETPLATFORMINFO clGetPlatformInfo;
OCL_CLGETPROGRAMBUILDINFO clGetProgramBuildInfo;
OCL_CLGETPROGRAMINFO clGetProgramInfo;
OpenCL Runtime: Workaround JiT compiler deadlock on NVIDIA driver >= 465.89
2021-04-11 11:35:40 +00:00
OCL_CLLINKPROGRAM clLinkProgram;
Get rid of exit() calls in OpenCL wrapper library with the goal to have a better control which error can be ignored under special circumstances Note, not all return codes from some of the subfunctions are uset yet, it would be too much changes at once This is a preparation for https://github.com/hashcat/hashcat/issues/416
2016-07-10 11:23:06 +00:00
OCL_CLRELEASECOMMANDQUEUE clReleaseCommandQueue;
OCL_CLRELEASECONTEXT clReleaseContext;
OCL_CLRELEASEEVENT clReleaseEvent;
OCL_CLRELEASEKERNEL clReleaseKernel;
OCL_CLRELEASEMEMOBJECT clReleaseMemObject;
OCL_CLRELEASEPROGRAM clReleaseProgram;
OCL_CLSETKERNELARG clSetKernelArg;
Add support for clUnloadPlatformCompiler()
2021-05-02 08:15:25 +00:00
OCL_CLUNLOADPLATFORMCOMPILER clUnloadPlatformCompiler;
Get rid of exit() calls in OpenCL wrapper library with the goal to have a better control which error can be ignored under special circumstances Note, not all return codes from some of the subfunctions are uset yet, it would be too much changes at once This is a preparation for https://github.com/hashcat/hashcat/issues/416
2016-07-10 11:23:06 +00:00
OCL_CLWAITFOREVENTS clWaitForEvents;
Initial commit
2015-12-04 14:47:52 +00:00
Implemented OpenCL library loader
2016-01-26 20:40:49 +00:00
} hc_opencl_lib_t;
Preparation for easier integration of: * https://github.com/hashcat/hashcat/pull/485 * https://github.com/hashcat/hashcat/pull/486
2016-09-05 19:47:26 +00:00
typedef hc_opencl_lib_t OCL_PTR;
Implemented OpenCL library loader
2016-01-26 20:40:49 +00:00
Get rid of exit() calls in OpenCL wrapper library with the goal to have a better control which error can be ignored under special circumstances Note, not all return codes from some of the subfunctions are uset yet, it would be too much changes at once This is a preparation for https://github.com/hashcat/hashcat/issues/416
2016-07-10 11:23:06 +00:00
const char *val2cstr_cl (cl_int CL_err);
Replace #pragma once with #ifndef #define #endif logic because #pragma once does not work cleanly on OSX
2016-09-06 16:44:05 +00:00
#endif // _EXT_OPENCL_H
Reference in New Issue Copy Permalink