22 MetalDeviceQueue(MetalDevice *device);
49 id<MTLBlitCommandEncoder> get_blit_encoder();
51 MetalDevice *metal_device_;
52 MetalBufferPool temp_buffer_pool_;
54 API_AVAILABLE(macos(11.0), ios(14.0))
55 MTLCommandBufferDescriptor *command_buffer_desc_ =
nullptr;
56 id<MTLDevice> mtlDevice_ = nil;
57 id<MTLCommandQueue> mtlCommandQueue_ = nil;
58 id<MTLCommandBuffer> mtlCommandBuffer_ = nil;
59 id<MTLComputeCommandEncoder> mtlComputeEncoder_ = nil;
60 id<MTLBlitCommandEncoder> mtlBlitEncoder_ = nil;
61 API_AVAILABLE(macos(10.14), ios(14.0))
62 id<MTLSharedEvent> shared_event_ = nil;
63 API_AVAILABLE(macos(10.14), ios(14.0))
64 MTLSharedEventListener *shared_event_listener_ = nil;
66 dispatch_queue_t event_queue_;
67 dispatch_semaphore_t wait_semaphore_;
74 std::vector<CopyBack> copy_back_mem_;
77 uint64_t command_buffers_submitted_ = 0;
78 uint64_t command_buffers_completed_ = 0;
81 void close_compute_encoder();
82 void close_blit_encoder();
84 bool verbose_tracing_ =
false;
85 bool label_command_encoders_ =
false;
94 std::vector<TimingData> command_encoder_labels_;
95 API_AVAILABLE(macos(10.14), ios(14.0))
96 id<MTLSharedEvent> timing_shared_event_ = nil;
98 uint64_t command_buffer_start_timing_id_;
101 double total_time = 0.0;
106 double last_completion_time_ = 0.0;
110 id<MTLCaptureScope> mtlCaptureScope_ = nil;
112 int capture_dispatch_counter_ = 0;
113 bool capture_samples_ =
false;
114 int capture_reset_counter_ = 0;
115 bool is_capturing_ =
false;
116 bool is_capturing_to_disk_ =
false;
117 bool has_captured_to_disk_ =
false;
static DBVT_INLINE btScalar size(const btDbvtVolume &a)
virtual int num_sort_partition_elements() const
virtual void copy_from_device(device_memory &mem)=0
virtual int num_concurrent_states(const size_t state_size) const =0
virtual void init_execution()=0
virtual void copy_to_device(device_memory &mem)=0
virtual int num_concurrent_busy_states() const =0
virtual bool synchronize()=0
virtual bool enqueue(DeviceKernel kernel, const int work_size, DeviceKernelArguments const &args)=0
virtual void zero_to_device(device_memory &mem)=0
#define CCL_NAMESPACE_END
SyclQueue void void size_t num_bytes SyclQueue void const char void *memory_device_pointer KernelContext int kernel
ccl_gpu_kernel_postfix ccl_global const int ccl_global float const int work_size
unsigned __int64 uint64_t