代码之家 › 专栏 › 技术社区 › einpoklum

ptxas抱怨我的sad设备功能的类型

ptx cuda

einpoklum · 技术社区 · 4 年前

//
// Generated by NVIDIA NVVM Compiler... sort of
//
// Compiler Build ID: CL-25769353
// Cuda compilation tools, release 10.1, V10.1.105
// Based on LLVM 3.4svn
//

.version 6.4
.target sm_30
.address_size 64

.func  (.param .b32 func_retval0) foo(
        .param .b32 foo_param_0,
        .param .b32 foo_param_1,
        .param .b32 foo_param_2
)
{
        .reg .b16       %rs<3>;
        .reg .b32       %r<3>;


        ld.param.u16    %rs1, [foo_param_0];
        ld.param.u16    %rs2, [foo_param_1];
        ld.param.u32    %r2, [foo_param_2];
        // inline asm
        sad.s16 %r1, %rs1, %rs2, %r2;
        // inline asm
        st.param.b32    [func_retval0+0], %r1;
        ret;
}

ptxas /tmp/a.ptx, line 27; error   : Arguments mismatch for instruction 'sad'
ptxas fatal   : Ptx assembly aborted due to errors

为什么?这种类型的组合有什么问题?

这个 PTX reference 说:

sad.type  d, a, b, c;

.type = { .u16, .u32, .u64,
          .s16, .s32, .s64 };

d 和 c u32 总是和 type 适用于 a 和 b . 这就是 __sad() 中的函数 device_functions.h

1 回复 | 直到 4 年前

einpoklum 4 年前

实际上 d a 需要是“类型的未签名版本” b c ". 所以,这应该是可行的:

.func  (.param .b32 func_retval0) foo(
        .param .b32 foo_param_0,
        .param .b32 foo_param_1,
        .param .b32 foo_param_2
)
{
        .reg .b32       %r<5>;


        ld.param.u32    %r4, [foo_param_2];
        ld.param.s16    %r2, [foo_param_0];
        ld.param.s16    %r3, [foo_param_1];
        // inline asm
        sad.s32 %r1, %r2, %r3, %r4;
        // inline asm
        st.param.b32    [func_retval0+0], %r1;
        ret;
}

推荐文章

Jacob Chang · 关于树约简中共享内存的问题

2 年前

yuanyesjtu · CUDA gpu矢量[重复]

6 年前

noobie2023 · 使用CUDA的前缀和

6 年前

Min · 在C++中,是否有“-Wl,-stack,[一个数字,例如4194304表示4Mb的堆栈]”的CUDA等价物?

6 年前

user3821901 · CUDA协作组:链接错误

6 年前

Utku Ufuk · CUDA错误:“\uu device\uuuu、\uu constant\uuuu和\uu shared\uuuu变量不支持动态初始化”

6 年前

Vandana · 将原始数据转换为推力中的复数向量

6 年前

user2330963 · 编译多个cuda文件(具有动态并行性)和MPI代码

6 年前

Farzad · 序列化CUfunction对象

6 年前

Vandana · 在以下矩阵副本内核中合并访问

6 年前