4040#include  " ggml-sycl/presets.hpp" 
4141#include  " ggml-sycl/gemm.hpp" 
4242
43- #define  UNUSED  GGML_UNUSED
44- 
4543static  bool  g_sycl_loaded = false ;
4644
4745static  ggml_sycl_device_info ggml_sycl_init () {
@@ -495,13 +493,13 @@ catch (sycl::exception const &exc) {
495493
496494static  size_t  ggml_backend_sycl_buffer_type_get_alignment (ggml_backend_buffer_type_t  buft) {
497495    return  128 ;
498-     UNUSED (buft);
496+     GGML_UNUSED (buft);
499497}
500498
501499static  size_t  ggml_backend_sycl_buffer_type_get_max_size (ggml_backend_buffer_type_t  buft) {
502500    return  dpct::get_current_device ().get_max_mem_alloc_size ();
503501
504-     UNUSED (buft);
502+     GGML_UNUSED (buft);
505503}
506504
507505static  size_t  ggml_backend_sycl_buffer_type_get_alloc_size (ggml_backend_buffer_type_t  buft, const  ggml_tensor * tensor) {
@@ -516,7 +514,7 @@ static size_t ggml_backend_sycl_buffer_type_get_alloc_size(ggml_backend_buffer_t
516514
517515    return  size;
518516
519-     UNUSED (buft);
517+     GGML_UNUSED (buft);
520518}
521519
522520static  const  ggml_backend_buffer_type_i ggml_backend_sycl_buffer_type_interface = {
@@ -703,7 +701,7 @@ struct ggml_backend_sycl_split_buffer_context {
703701static  const  char  * ggml_backend_sycl_split_buffer_get_name (ggml_backend_buffer_t  buffer) {
704702    return  GGML_SYCL_NAME " _Split"  ;
705703
706-     UNUSED (buffer);
704+     GGML_UNUSED (buffer);
707705}
708706
709707static  bool  ggml_backend_buffer_is_sycl_split (ggml_backend_buffer_t  buffer) {
@@ -719,7 +717,7 @@ static void * ggml_backend_sycl_split_buffer_get_base(ggml_backend_buffer_t buff
719717    //  the pointers are stored in the tensor extras, this is just a dummy address and never dereferenced
720718    return  (void  *)0x1000 ;
721719
722-     UNUSED (buffer);
720+     GGML_UNUSED (buffer);
723721}
724722
725723static  void 
@@ -912,8 +910,8 @@ catch (sycl::exception const &exc) {
912910}
913911
914912static  void  ggml_backend_sycl_split_buffer_clear (ggml_backend_buffer_t  buffer, uint8_t  value) {
915-     UNUSED (buffer);
916-     UNUSED (value);
913+     GGML_UNUSED (buffer);
914+     GGML_UNUSED (value);
917915}
918916
919917static  struct  ggml_backend_buffer_i  ggml_backend_sycl_split_buffer_interface = {
@@ -934,7 +932,7 @@ static struct ggml_backend_buffer_i ggml_backend_sycl_split_buffer_interface = {
934932static  const  char  * ggml_backend_sycl_split_buffer_type_get_name (ggml_backend_buffer_type_t  buft) {
935933    return  GGML_SYCL_NAME " _Split"  ;
936934
937-     UNUSED (buft);
935+     GGML_UNUSED (buft);
938936}
939937
940938static  ggml_backend_buffer_t  ggml_backend_sycl_split_buffer_type_alloc_buffer (ggml_backend_buffer_type_t  buft, size_t  size) {
@@ -949,7 +947,7 @@ static ggml_backend_buffer_t ggml_backend_sycl_split_buffer_type_alloc_buffer(gg
949947
950948static  size_t  ggml_backend_sycl_split_buffer_type_get_alignment (ggml_backend_buffer_type_t  buft) {
951949    return  128 ;
952-     UNUSED (buft);
950+     GGML_UNUSED (buft);
953951}
954952
955953static  size_t  ggml_backend_sycl_split_buffer_type_get_alloc_size (ggml_backend_buffer_type_t  buft, const  ggml_tensor * tensor) {
@@ -982,7 +980,7 @@ static size_t ggml_backend_sycl_split_buffer_type_get_alloc_size(ggml_backend_bu
982980static  bool  ggml_backend_sycl_split_buffer_type_is_host (ggml_backend_buffer_type_t  buft) {
983981    return  false ;
984982
985-     UNUSED (buft);
983+     GGML_UNUSED (buft);
986984}
987985
988986static  ggml_backend_buffer_type_i ggml_backend_sycl_split_buffer_type_interface = {
@@ -1039,13 +1037,13 @@ ggml_backend_buffer_type_t ggml_backend_sycl_split_buffer_type(const float * ten
10391037static  const  char  * ggml_backend_sycl_host_buffer_type_name (ggml_backend_buffer_type_t  buft) {
10401038    return  GGML_SYCL_NAME " _Host"  ;
10411039
1042-     UNUSED (buft);
1040+     GGML_UNUSED (buft);
10431041}
10441042
10451043static  const  char  * ggml_backend_sycl_host_buffer_name (ggml_backend_buffer_t  buffer) {
10461044    return  GGML_SYCL_NAME " _Host"  ;
10471045
1048-     UNUSED (buffer);
1046+     GGML_UNUSED (buffer);
10491047}
10501048
10511049static  void  ggml_backend_sycl_host_buffer_free_buffer (ggml_backend_buffer_t  buffer) {
@@ -4962,7 +4960,7 @@ static void ggml_backend_sycl_synchronize(ggml_backend_t backend) try {
49624960    const  queue_ptr stream = sycl_ctx->stream (sycl_ctx->device , 0 );
49634961    SYCL_CHECK (CHECK_TRY_ERROR ((stream)->wait ()));
49644962
4965-     UNUSED (backend);
4963+     GGML_UNUSED (backend);
49664964}
49674965catch  (sycl::exception const  &exc) {
49684966  std::cerr << exc.what () << " Exception caught at file:"   << __FILE__
@@ -5117,11 +5115,12 @@ static void ggml_backend_sycl_device_get_props(ggml_backend_dev_t dev, ggml_back
51175115#else 
51185116    bool  events = true ;
51195117#endif 
5118+ 
51205119    props->caps  = {
5121-         /*  async       */   true ,
5122-         /*  host_buffer */   host_buffer,
5120+         /*  . async                 =  */   true ,
5121+         /*  . host_buffer           =  */   host_buffer,
51235122        /*  .buffer_from_host_ptr  = */   false ,
5124-         /*  events      */   events,
5123+         /*  . events                =  */   events,
51255124    };
51265125}
51275126
@@ -5293,7 +5292,7 @@ static bool ggml_backend_sycl_device_supports_op(ggml_backend_dev_t dev, const g
52935292            return  false ;
52945293    }
52955294
5296-     UNUSED (dev);
5295+     GGML_UNUSED (dev);
52975296}
52985297
52995298static  bool  ggml_backend_sycl_device_supports_buft (ggml_backend_dev_t  dev, ggml_backend_buffer_type_t  buft) {
0 commit comments