<html>
<head>
<base href="https://bugs.llvm.org/">
</head>
<body><table border="1" cellspacing="0" cellpadding="8">
<tr>
<th>Bug ID</th>
<td><a class="bz_bug_link
bz_status_NEW "
title="NEW - The __m64 not passed according to i386 ABI"
href="https://bugs.llvm.org/show_bug.cgi?id=41029">41029</a>
</td>
</tr>
<tr>
<th>Summary</th>
<td>The __m64 not passed according to i386 ABI
</td>
</tr>
<tr>
<th>Product</th>
<td>clang
</td>
</tr>
<tr>
<th>Version</th>
<td>trunk
</td>
</tr>
<tr>
<th>Hardware</th>
<td>PC
</td>
</tr>
<tr>
<th>OS</th>
<td>Linux
</td>
</tr>
<tr>
<th>Status</th>
<td>NEW
</td>
</tr>
<tr>
<th>Severity</th>
<td>normal
</td>
</tr>
<tr>
<th>Priority</th>
<td>P
</td>
</tr>
<tr>
<th>Component</th>
<td>LLVM Codegen
</td>
</tr>
<tr>
<th>Assignee</th>
<td>unassignedclangbugs@nondot.org
</td>
</tr>
<tr>
<th>Reporter</th>
<td>wei3.xiao@intel.com
</td>
</tr>
<tr>
<th>CC</th>
<td>llvm-bugs@lists.llvm.org, neeilans@live.com, richard-llvm@metafoo.co.uk
</td>
</tr></table>
<p>
<div>
<pre>$ cat m64.c
#include <immintrin.h>
void callee(__m64 __m1, __m64 __m2);
__m64 caller(__m64 __m1, __m64 __m2)
{
__m64 a = _mm_set_pi16(1, 2, 3, 4);
callee(__m2, __m1);
return a;
}
$ gcc -m32 -O2 -S -o - m64.c
.file "m64.c"
.text
.p2align 4
.globl caller
.type caller, @function
caller:
.LFB5121:
.cfi_startproc
subl $12, %esp
.cfi_def_cfa_offset 16
movq %mm0, %mm2
movq %mm1, %mm0
movq %mm2, %mm1
call callee
movq .LC0, %mm0
addl $12, %esp
.cfi_def_cfa_offset 4
ret
.cfi_endproc
.LFE5121:
.size caller, .-caller
.section .rodata.cst8,"aM",@progbits,8
.align 8
.LC0:
.value 4
.value 3
.value 2
.value 1
.ident "GCC: (GNU) 9.0.1 20190131 (experimental)"
.section .note.GNU-stack,"",@progbits
$ clang -m32 -O2 -S -o - m64.c
.text
.file "m64.c"
.globl caller # -- Begin function caller
.p2align 4, 0x90
.type caller,@function
caller: # @caller
# %bb.0: # %entry
subl $12, %esp
pushl 20(%esp)
pushl 20(%esp)
pushl 36(%esp)
pushl 36(%esp)
calll callee
addl $16, %esp
movl $196612, %eax # imm = 0x30004
movl $65538, %edx # imm = 0x10002
addl $12, %esp
retl
.Lfunc_end0:
.size caller, .Lfunc_end0-caller
# -- End function
.ident "clang version 9.0.0 (<a href="http://llvm.org/git/clang.git">http://llvm.org/git/clang.git</a>
59f2009cd157fc96a0d558125405b98586cd83d2) (<a href="http://llvm.org/git/llvm.git">http://llvm.org/git/llvm.git</a>
6a7719c7965af52f904e16588c1754f65bcb8ff0)"
.section ".note.GNU-stack","",@progbits
.addrsig
According to i386 ABI, __m64 values should be passed by mmx registers.</pre>
</div>
</p>
<hr>
<span>You are receiving this mail because:</span>
<ul>
<li>You are on the CC list for the bug.</li>
</ul>
</body>
</html>