[ROCm][Windows] Fixing undefined symbol linker error after exposing MIOpen symbols (#2415)

Changing TORCH_CUDA_CPP_API macros to TORCH_HIP_CPP in MIOpen header
files according to closed
[PR](pytorch#156479) in pytorch
upstream.

---------

Signed-off-by: Jagadish Krishnamoorthy <[email protected]>
Co-authored-by: Jithun Nair <[email protected]>
Co-authored-by: Ethan Wee <[email protected]>
Co-authored-by: Jithun Nair <[email protected]>
Co-authored-by: Xinya Zhang <[email protected]>
Co-authored-by: Prachi Gupta <[email protected]>
Co-authored-by: Dmitry Nikolaev <[email protected]>
Co-authored-by: iupaikov-amd <[email protected]>
Co-authored-by: omkar kakarparthi <[email protected]>
Co-authored-by: Jeff Daily <[email protected]>
Co-authored-by: rocm-mici <[email protected]>
Co-authored-by: Michael Halkenhäuser <[email protected]>
Co-authored-by: Hashem Hashemi <[email protected]>
Co-authored-by: Jagadish Krishnamoorthy <[email protected]>
Co-authored-by: Andres Lugo <[email protected]>
Co-authored-by: pmaybank <[email protected]>
Co-authored-by: pnikolic-amd <[email protected]>
Co-authored-by: Jerry Mannil <[email protected]>
Co-authored-by: Sampsa Riikonen <[email protected]>
Co-authored-by: Ramya Ramineni <[email protected]>
Co-authored-by: pytorchbot <[email protected]>
Co-authored-by: Nikita Shulga <[email protected]>
Co-authored-by: rzou <[email protected]>
Co-authored-by: atalman <[email protected]>
Co-authored-by: David Berard <[email protected]>
Co-authored-by: Frank Lin <[email protected]>
Co-authored-by: Wei Wang <[email protected]>
Co-authored-by: Cao E <[email protected]>
Co-authored-by: Sidharth Subbarao <[email protected]>
Co-authored-by: Camyll Harajli <[email protected]>
Co-authored-by: Aditya Tewari <[email protected]>
Co-authored-by: Christopher Sidebottom <[email protected]>
Co-authored-by: Ryo Suzuki <[email protected]>
Co-authored-by: Ye Tao <[email protected]>
Co-authored-by: Nikita Shulga <[email protected]>
Co-authored-by: Eli Uriegas <[email protected]>
Co-authored-by: Luca Wehrstedt <[email protected]>
Co-authored-by: Robert Hardwick <[email protected]>
Co-authored-by: Svetlana Karslioglu <[email protected]>
Co-authored-by: Michael Lazos <[email protected]>
Co-authored-by: bobrenjc93 <[email protected]>
Co-authored-by: Nikita Shulga <[email protected]>
Co-authored-by: Jane Xu <[email protected]>
Co-authored-by: charlifu <[email protected]>
Co-authored-by: Jack Taylor <[email protected]>
Co-authored-by: Nichols A. Romero <[email protected]>
Co-authored-by: Copilot <[email protected]>
Co-authored-by: Sriram Kumar <[email protected]>
Co-authored-by: Divin Honnappa <[email protected]>
Co-authored-by: akashveramd <[email protected]>

Author: 47 people

aten/src/ATen/miopen/Descriptors.h

@@ -39,7 +39,7 @@ struct DescriptorDeleter {
 // function.
 template <typename T, miopenStatus_t (*ctor)(T**), miopenStatus_t (*dtor)(T*)>
 // NOLINTNEXTLINE(bugprone-exception-escape)
-class TORCH_CUDA_CPP_API Descriptor {
+class TORCH_HIP_CPP_API Descriptor {
  public:
   // Use desc() to access the underlying descriptor pointer in
   // a read-only fashion.  Most client code should use this.
@@ -65,7 +65,7 @@ class TORCH_CUDA_CPP_API Descriptor {
   std::unique_ptr<T, DescriptorDeleter<T, dtor>> desc_;
 };
 
-class TORCH_CUDA_CPP_API TensorDescriptor : public Descriptor<
+class TORCH_HIP_CPP_API TensorDescriptor : public Descriptor<
                                                miopenTensorDescriptor,
                                                &miopenCreateTensorDescriptor,
                                                &miopenDestroyTensorDescriptor> {
@@ -88,7 +88,7 @@ class TORCH_CUDA_CPP_API TensorDescriptor : public Descriptor<
 
 std::ostream& operator<<(std::ostream & out, const TensorDescriptor& d);
 
-class TORCH_CUDA_CPP_API FilterDescriptor : public Descriptor<
+class TORCH_HIP_CPP_API FilterDescriptor : public Descriptor<
                                                miopenTensorDescriptor,
                                                &miopenCreateTensorDescriptor,
                                                &miopenDestroyTensorDescriptor> {
@@ -105,7 +105,7 @@ class TORCH_CUDA_CPP_API FilterDescriptor : public Descriptor<
   }
 };
 
-struct TORCH_CUDA_CPP_API ConvolutionDescriptor
+struct TORCH_HIP_CPP_API ConvolutionDescriptor
     : public Descriptor<
           miopenConvolutionDescriptor,
           &miopenCreateConvolutionDescriptor,
@@ -121,7 +121,7 @@ struct TORCH_CUDA_CPP_API ConvolutionDescriptor
 };
 
 // NOLINTNEXTLINE(bugprone-exception-escape)
-struct TORCH_CUDA_CPP_API DropoutDescriptor
+struct TORCH_HIP_CPP_API DropoutDescriptor
     : public Descriptor<
           miopenDropoutDescriptor,
           &miopenCreateDropoutDescriptor,
@@ -137,7 +137,7 @@ struct TORCH_CUDA_CPP_API DropoutDescriptor
     }
 };
 
-struct TORCH_CUDA_CPP_API RNNDescriptor
+struct TORCH_HIP_CPP_API RNNDescriptor
   : public Descriptor<miopenRNNDescriptor,
                       &miopenCreateRNNDescriptor,
                       &miopenDestroyRNNDescriptor>

aten/src/ATen/miopen/Handle.h

@@ -5,5 +5,5 @@
 
 namespace at::native {
 
-TORCH_CUDA_CPP_API miopenHandle_t getMiopenHandle();
+TORCH_HIP_CPP_API miopenHandle_t getMiopenHandle();
 } // namespace at::native

aten/src/ATen/miopen/Types.h

@@ -6,7 +6,7 @@
 
 namespace at::native {
 
-TORCH_CUDA_CPP_API miopenDataType_t getMiopenDataType(const at::Tensor& tensor);
+TORCH_HIP_CPP_API miopenDataType_t getMiopenDataType(const at::Tensor& tensor);
 
 int64_t miopen_version();