torch_utils.h 2.63 KB
Newer Older
traveller59's avatar
traveller59 committed
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
// Copyright 2019 Yan Yan
// 
// Licensed under the Apache License, Version 2.0 (the "License");
// you may not use this file except in compliance with the License.
// You may obtain a copy of the License at
// 
//     http://www.apache.org/licenses/LICENSE-2.0
// 
// Unless required by applicable law or agreed to in writing, software
// distributed under the License is distributed on an "AS IS" BASIS,
// WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
// See the License for the specific language governing permissions and
// limitations under the License.

#pragma once
#include <tensorview/tensorview.h>
#include <torch/script.h>
#include <ATen/ATen.h>
traveller59's avatar
traveller59 committed
19
#ifdef SPCONV_CUDA
traveller59's avatar
traveller59 committed
20
#include <ATen/cuda/CUDAContext.h>
traveller59's avatar
traveller59 committed
21
#endif
traveller59's avatar
traveller59 committed
22
23

namespace tv {
traveller59's avatar
traveller59 committed
24
25
  
#ifdef SPCONV_CUDA
traveller59's avatar
traveller59 committed
26
struct TorchGPU: public tv::GPU {
27
28
  virtual cudaStream_t getStream() const override {
    return at::cuda::getCurrentCUDAStream();
traveller59's avatar
traveller59 committed
29
30
  }
};
traveller59's avatar
traveller59 committed
31
#endif
traveller59's avatar
traveller59 committed
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
template <typename T> void check_torch_dtype(const torch::Tensor &tensor) {
  switch (tensor.type().scalarType()) {
  case at::ScalarType::Double: {
    auto val = std::is_same<std::remove_const_t<T>, double>::value;
    TV_ASSERT_RT_ERR(val, "error");
    break;
  }
  case at::ScalarType::Float: {
    auto val = std::is_same<std::remove_const_t<T>, float>::value;
    TV_ASSERT_RT_ERR(val, "error");
    break;
  }
  case at::ScalarType::Int: {
    auto val = std::is_same<std::remove_const_t<T>, int>::value;
    TV_ASSERT_RT_ERR(val, "error");
    break;
  }
  case at::ScalarType::Half: {
    auto val = std::is_same<std::remove_const_t<T>, at::Half>::value;
    TV_ASSERT_RT_ERR(val, "error");
    break;
  }
54
55
56
57
58
  case at::ScalarType::Long: {
    auto val = std::is_same<std::remove_const_t<T>, long>::value;
    TV_ASSERT_RT_ERR(val, "error");
    break;
  }
traveller59's avatar
traveller59 committed
59
60
61
62
63
  default:
    TV_ASSERT_RT_ERR(false, "error");
  }
}

64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
template <typename T>
constexpr auto type2torch(T val=T()) -> decltype(torch::kInt32){
  TV_ASSERT_RT_ERR(false, "unknown type");
}

template <>
constexpr auto type2torch(int val) -> decltype(torch::kInt32){
  return torch::kInt32;
}

template <>
constexpr auto type2torch(long val) -> decltype(torch::kInt32){
  return torch::kInt64;
}

template <>
constexpr auto type2torch(float val) -> decltype(torch::kInt32){
  return torch::kFloat32;
}

template <>
constexpr auto type2torch(double val) -> decltype(torch::kInt32){
  return torch::kFloat64;
}

traveller59's avatar
traveller59 committed
89
90
91
92
93
94
95
template <typename T>
tv::TensorView<T> torch2tv(const torch::Tensor &tensor) {
  check_torch_dtype<T>(tensor);
  tv::Shape shape;
  for (auto i : tensor.sizes()) {
    shape.push_back(i);
  }
traveller59's avatar
traveller59 committed
96
  return tv::TensorView<T>(tensor.data_ptr<std::remove_const_t<T>>(), shape);
traveller59's avatar
traveller59 committed
97
98
}
} // namespace tv