diff options
| author |  Yifei Feng <yifeif@google.com> | 2018-07-02 17:41:04 -0700 |
|---|---|---|
| committer | Yifei Feng <yifeif@google.com> | 2018-07-02 17:41:04 -0700 |
| commit | bf6ce077c426f2aa28034cf7ff6abff338dba63d (patch) | |
| tree | a0629b6e3531b1ea214430d8d97a56d2e86b4305 /tensorflow/stream_executor | |
| parent | 16a965c5c9a64ef82ccfcb849dd61e6aad00d10e (diff) | |
| parent | 4e55e566e17e5cbef4db8d86df5ea22c244c7031 (diff) | |
Merge commit for internal changes
Diffstat (limited to 'tensorflow/stream_executor')
| -rw-r--r-- | tensorflow/stream_executor/cuda/cuda_dnn.cc | 16 |
1 files changed, 16 insertions, 0 deletions
diff --git a/tensorflow/stream_executor/cuda/cuda_dnn.cc b/tensorflow/stream_executor/cuda/cuda_dnn.cc index d4f2fd2625..84916385a8 100644 --- a/tensorflow/stream_executor/cuda/cuda_dnn.cc +++ b/tensorflow/stream_executor/cuda/cuda_dnn.cc @@ -3074,6 +3074,22 @@ port::Status CudnnSupport::DoConvolveBackwardDataImpl( } } + // Cudnn 7.1.4 has a bug if the workspace of the following convolution is not + // zero-initialized. + // TODO(timshen): Add an nvbugs/ link. + if (CUDNN_VERSION >= 7000 && + algorithm_config.algorithm().algo_id() == + CUDNN_CONVOLUTION_BWD_DATA_ALGO_1 && + cudnn_type == CUDNN_DATA_HALF && + algorithm_config.algorithm().tensor_ops_enabled() && + input_descriptor.layout() == dnn::DataLayout::kBatchYXDepth && + filter_descriptor.layout() == dnn::FilterLayout::kOutputInputYX && + output_descriptor.layout() == dnn::DataLayout::kBatchDepthYX && + (convolution_descriptor.vertical_filter_stride() > 1 || + convolution_descriptor.horizontal_filter_stride() > 1)) { + stream->ThenMemZero(&scratch, scratch.size()); + } + RETURN_IF_CUDNN_ERROR( cudnnConvolutionBackwardData(cudnn.handle(), /*alpha=*/alpha, |