mirror-ac/driver/driver.h

#ifndef DRIVER_H
#define DRIVER_H

#include "common.h"

#include <wdf.h>

#include "modules.h"
#include "integrity.h"
#include "callbacks.h"

#include "containers/map.h"
#include "containers/tree.h"

BCRYPT_ALG_HANDLE*
GetCryptHandle_AES();

BCRYPT_ALG_HANDLE*
GetCryptHandle_Sha256();

NTSTATUS
QueryActiveApcContextsForCompletion();

LPCSTR
GetDriverName();

PDEVICE_OBJECT
GetDriverDeviceObject();

PDRIVER_OBJECT
GetDriverObject();

PIRP_QUEUE_HEAD
GetIrpQueueHead();

PSYS_MODULE_VAL_CONTEXT
GetSystemModuleValidationContext();

PUNICODE_STRING
GetDriverPath();

PUNICODE_STRING
GetDriverRegistryPath();

PUNICODE_STRING
GetDriverDeviceName();

PUNICODE_STRING
GetDriverSymbolicLink();

PSYSTEM_INFORMATION
GetDriverConfigSystemInformation();

PRB_TREE
GetThreadTree();

PDRIVER_LIST_HEAD
GetDriverList();

PUINT64
GetApcContextArray();

VOID
AcquireDriverConfigLock();

VOID
ReleaseDriverConfigLock();

BOOLEAN
IsDriverUnloading();

PACTIVE_SESSION
GetActiveSession();

PSHARED_MAPPING
GetSharedMappingConfig();

VOID
UnsetNmiInProgressFlag();

BOOLEAN
IsNmiInProgress();

BOOLEAN
HasDriverLoaded();

PRTL_HASHMAP
GetProcessHashmap();

__m256i*
GetDriverImportsKey();

PUINT64
GetDriverDeviceExtensionKey();

#endif