Skip to content

Commit 9030d62

Browse files
committed
* lint error
1 parent 597a945 commit 9030d62

File tree

4 files changed

+24
-24
lines changed

4 files changed

+24
-24
lines changed

src/runtime/c_runtime_api.cc

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -171,7 +171,7 @@ void* DeviceAPI::AllocDataSpace(Device dev, int ndim, const int64_t* shape, DLDa
171171
return nullptr;
172172
}
173173

174-
void * DeviceAPI::GetNativePtr(Device dev, void *ptr) { return nullptr; }
174+
void* DeviceAPI::GetNativePtr(Device dev, void* ptr) { return nullptr; }
175175

176176
void DeviceAPI::CopyDataFromTo(DLTensor* from, DLTensor* to, TVMStreamHandle stream) {
177177
// by default, we can always redirect to the flat memory copy operation.

src/runtime/opencl/opencl_common.h

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -313,7 +313,7 @@ class OpenCLWorkspace : public DeviceAPI {
313313

314314
void CopyDataFromTo(DLTensor* from, DLTensor* to, TVMStreamHandle stream) final;
315315

316-
void* CreateHostPtrIfEnabled(BufferDescriptor *desc, Device dev, size_t size);
316+
void* CreateHostPtrIfEnabled(BufferDescriptor* desc, Device dev, size_t size);
317317
};
318318

319319
/*! \brief Thread local workspace */
@@ -375,7 +375,7 @@ struct BufferDescriptor {
375375
static String ScopeFromMemoryLayout(MemoryLayout mem_scope);
376376

377377
cl_mem buffer{nullptr};
378-
cl_uchar *host_ptr{nullptr};
378+
cl_uchar* host_ptr{nullptr};
379379
MemoryLayout layout{MemoryLayout::kBuffer1D};
380380
};
381381
} // namespace cl

src/runtime/opencl/opencl_device_api.cc

Lines changed: 11 additions & 11 deletions
Original file line numberDiff line numberDiff line change
@@ -28,7 +28,7 @@
2828
#include "opencl_common.h"
2929

3030
#ifdef OPENCL_ENABLE_HOST_PTR
31-
#define CL_MEM_CREATE_FLAGS CL_MEM_READ_WRITE|CL_MEM_ALLOC_HOST_PTR
31+
#define CL_MEM_CREATE_FLAGS CL_MEM_READ_WRITE | CL_MEM_ALLOC_HOST_PTR
3232
#else
3333
#define CL_MEM_CREATE_FLAGS CL_MEM_READ_WRITE
3434
#endif
@@ -203,15 +203,15 @@ void OpenCLWorkspace::GetAttr(Device dev, DeviceAttrKind kind, TVMRetValue* rv)
203203
}
204204
}
205205

206-
void * OpenCLWorkspace::CreateHostPtrIfEnabled(cl::BufferDescriptor* desc, Device dev, size_t size) {
206+
void* OpenCLWorkspace::CreateHostPtrIfEnabled(cl::BufferDescriptor* desc, Device dev, size_t size) {
207207
#if defined(OPENCL_ENABLE_HOST_PTR)
208-
cl_int err_code;
209-
desc->host_ptr = (cl_uchar *)clEnqueueMapBuffer(this->GetQueue(dev), desc->buffer, CL_TRUE,
210-
CL_MAP_WRITE, 0, sizeof(cl_uchar) * size, 0,
211-
NULL, NULL, &err_code);
212-
OPENCL_CHECK_ERROR(err_code);
208+
cl_int err_code;
209+
desc->host_ptr = reinterpret_cast<cl_uchar*>(
210+
clEnqueueMapBuffer(this->GetQueue(dev), desc->buffer, CL_TRUE, CL_MAP_WRITE, 0,
211+
sizeof(cl_uchar) * size, 0, NULL, NULL, &err_code));
212+
OPENCL_CHECK_ERROR(err_code);
213213
#endif // OPENCL_ENABLE_HOST_PTR
214-
return desc;
214+
return desc;
215215
}
216216

217217
void* OpenCLWorkspace::AllocDataSpace(Device dev, size_t size, size_t alignment,
@@ -260,9 +260,9 @@ void OpenCLWorkspace::FreeDataSpace(Device dev, void* ptr) {
260260
OPENCL_CALL(clFinish(this->GetQueue(dev)));
261261

262262
cl::BufferDescriptor* desc = static_cast<cl::BufferDescriptor*>(ptr);
263-
if(desc->host_ptr) {
264-
clEnqueueUnmapMemObject(this->GetQueue(dev), desc->buffer, (void *) desc->host_ptr, 0, NULL,
265-
NULL);
263+
if (desc->host_ptr) {
264+
clEnqueueUnmapMemObject(this->GetQueue(dev), desc->buffer,
265+
reinterpret_cast<void*>(desc->host_ptr), 0, NULL, NULL);
266266
}
267267
OPENCL_CALL(clReleaseMemObject(desc->buffer));
268268
delete desc;

src/runtime/opencl/opencl_wrapper/opencl_wrapper.cc

Lines changed: 10 additions & 10 deletions
Original file line numberDiff line numberDiff line change
@@ -173,10 +173,10 @@ using f_clEnqueueNDRangeKernel = cl_int (*)(cl_command_queue, cl_kernel, cl_uint
173173
cl_event*);
174174
using f_clCreateCommandQueue = cl_command_queue (*)(cl_context, cl_device_id,
175175
cl_command_queue_properties, cl_int*);
176-
using f_clEnqueueUnmapMemObject = cl_int (*)(cl_command_queue, cl_mem, void*,
177-
cl_uint, const cl_event*, cl_event*);
178-
using f_clEnqueueMapBuffer = void * (*) (cl_command_queue, cl_mem, cl_bool, cl_map_flags, size_t,
179-
size_t, cl_uint, const cl_event *, cl_event *, cl_int *);
176+
using f_clEnqueueUnmapMemObject = cl_int (*)(cl_command_queue, cl_mem, void*, cl_uint,
177+
const cl_event*, cl_event*);
178+
using f_clEnqueueMapBuffer = void* (*)(cl_command_queue, cl_mem, cl_bool, cl_map_flags, size_t,
179+
size_t, cl_uint, const cl_event*, cl_event*, cl_int*);
180180

181181
} // namespace
182182

@@ -590,15 +590,15 @@ cl_int clEnqueueUnmapMemObject(cl_command_queue queue, cl_mem memobj, void* mapp
590590
}
591591
}
592592

593-
void * clEnqueueMapBuffer (cl_command_queue command_queue, cl_mem buffer, cl_bool blocking_map,
594-
cl_map_flags map_flags, size_t offset, size_t cb,
595-
cl_uint num_events_in_wait_list, const cl_event *event_wait_list,
596-
cl_event *event, cl_int *errcode_ret) {
593+
void* clEnqueueMapBuffer(cl_command_queue command_queue, cl_mem buffer, cl_bool blocking_map,
594+
cl_map_flags map_flags, size_t offset, size_t cb,
595+
cl_uint num_events_in_wait_list, const cl_event* event_wait_list,
596+
cl_event* event, cl_int* errcode_ret) {
597597
auto& lib = LibOpenCLWrapper::getInstance();
598598
auto func = (f_clEnqueueMapBuffer)lib.getOpenCLFunction("clEnqueueMapBuffer");
599599
if (func) {
600-
return func(command_queue, buffer, blocking_map, map_flags, offset, cb,
601-
num_events_in_wait_list, event_wait_list, event, errcode_ret);
600+
return func(command_queue, buffer, blocking_map, map_flags, offset, cb, num_events_in_wait_list,
601+
event_wait_list, event, errcode_ret);
602602
} else {
603603
return nullptr;
604604
}

0 commit comments

Comments
 (0)