#include "deformableconv2d.h"
#include "fused_activation.h"
namespace ncnn {
DeformableConv2D::DeformableConv2D()
{
one_blob_only = false;
support_inplace = false;
}
int DeformableConv2D::load_param(const ParamDict& pd)
{
num_output = pd.get(0, 0);
kernel_w = pd.get(1, 0);
kernel_h = pd.get(11, kernel_w);
dilation_w = pd.get(2, 1);
dilation_h = pd.get(12, dilation_w);
stride_w = pd.get(3, 1);
stride_h = pd.get(13, stride_w);
pad_left = pd.get(4, 0);
pad_right = pd.get(15, pad_left);
pad_top = pd.get(14, pad_left);
pad_bottom = pd.get(16, pad_top);
bias_term = pd.get(5, 0);
weight_data_size = pd.get(6, 0);
activation_type = pd.get(9, 0);
activation_params = pd.get(10, Mat());
return 0;
}
int DeformableConv2D::load_model(const ModelBin& mb)
{
weight_data = mb.load(weight_data_size, 0);
if (weight_data.empty())
return -100;
if (bias_term)
{
bias_data = mb.load(num_output, 1);
if (bias_data.empty())
return -100;
}
return 0;
}
int DeformableConv2D::forward(const std::vector<Mat>& bottom_blobs, std::vector<Mat>& top_blobs, const Option& opt) const
{
const Mat& bottom_blob = bottom_blobs[0];
const Mat& offset = bottom_blobs[1];
const bool has_mask = (bottom_blobs.size() == 3);
const int w = bottom_blob.w;
const int h = bottom_blob.h;
const int in_c = bottom_blob.c;
const size_t elemsize = bottom_blob.elemsize;
const int kernel_extent_w = dilation_w * (kernel_w - 1) + 1;
const int kernel_extent_h = dilation_h * (kernel_h - 1) + 1;
const int out_w = (w + pad_left + pad_right - kernel_extent_w) / stride_w + 1;
const int out_h = (h + pad_top + pad_bottom - kernel_extent_h) / stride_h + 1;
Mat& output = top_blobs[0];
output.create(out_w, out_h, num_output, elemsize, opt.blob_allocator);
if (output.empty())
return -100;
const float* weight_ptr = weight_data;
const float* bias_ptr = weight_data;
if (bias_term)
bias_ptr = bias_data;
#pragma omp parallel for num_threads(opt.num_threads)
for (int h_col = 0; h_col < out_h; h_col++)
{
for (int w_col = 0; w_col < out_w; w_col++)
{
int h_in = h_col * stride_h - pad_top;
int w_in = w_col * stride_w - pad_left;
for (int oc = 0; oc < num_output; oc++)
{
float sum = 0.f;
if (bias_term)
sum = bias_ptr[oc];
for (int i = 0; i < kernel_h; i++)
{
for (int j = 0; j < kernel_w; j++)
{
const float offset_h = offset.channel((i * kernel_w + j) * 2).row(h_col)[w_col];
const float offset_w = offset.channel((i * kernel_w + j) * 2 + 1).row(h_col)[w_col];
const float mask_ = has_mask ? bottom_blobs[2].channel(i * kernel_w + j).row(h_col)[w_col] : 1.f;
const float h_im = h_in + i * dilation_h + offset_h;
const float w_im = w_in + j * dilation_w + offset_w;
const bool cond = h_im > -1 && w_im > -1 && h_im < h && w_im < w;
int h_low = 0;
int w_low = 0;
int h_high = 0;
int w_high = 0;
float w1 = 0.f;
float w2 = 0.f;
float w3 = 0.f;
float w4 = 0.f;
bool v1_cond = false;
bool v2_cond = false;
bool v3_cond = false;
bool v4_cond = false;
if (cond)
{
h_low = (int)floorf(h_im);
w_low = (int)floorf(w_im);
h_high = h_low + 1;
w_high = w_low + 1;
float lh = h_im - h_low;
float lw = w_im - w_low;
float hh = 1 - lh;
float hw = 1 - lw;
v1_cond = (h_low >= 0 && w_low >= 0);
v2_cond = (h_low >= 0 && w_high <= w - 1);
v3_cond = (h_high <= h - 1 && w_low >= 0);
v4_cond = (h_high <= h - 1 && w_high <= w - 1);
w1 = hh * hw;
w2 = hh * lw;
w3 = lh * hw;
w4 = lh * lw;
}
for (int c_im = 0; c_im < in_c; c_im++)
{
float val = 0.f;
if (cond)
{
float v1 = v1_cond ? bottom_blob.channel(c_im).row(h_low)[w_low] : 0.f;
float v2 = v2_cond ? bottom_blob.channel(c_im).row(h_low)[w_high] : 0.f;
float v3 = v3_cond ? bottom_blob.channel(c_im).row(h_high)[w_low] : 0.f;
float v4 = v4_cond ? bottom_blob.channel(c_im).row(h_high)[w_high] : 0.f;
val = w1 * v1 + w2 * v2 + w3 * v3 + w4 * v4;
}
sum += val * mask_ * weight_ptr[((oc * in_c + c_im) * kernel_h + i) * kernel_w + j];
}
}
}
output.channel(oc).row(h_col)[w_col] = activation_ss(sum, activation_type, activation_params);
}
}
}
return 0;
}
}