Lines Matching refs:zmm
178 regs->lr_vector[i].zmm[0] in pltenter()
181 __m512i zmm = _mm512_set1_epi64 (-1); in pltenter() local
182 asm volatile ("vmovdqa64 %0, %%zmm0" : : "x" (zmm) : "xmm0" ); in pltenter()
183 asm volatile ("vmovdqa64 %0, %%zmm1" : : "x" (zmm) : "xmm1" ); in pltenter()
184 asm volatile ("vmovdqa64 %0, %%zmm2" : : "x" (zmm) : "xmm2" ); in pltenter()
185 asm volatile ("vmovdqa64 %0, %%zmm3" : : "x" (zmm) : "xmm3" ); in pltenter()
186 asm volatile ("vmovdqa64 %0, %%zmm4" : : "x" (zmm) : "xmm4" ); in pltenter()
187 asm volatile ("vmovdqa64 %0, %%zmm5" : : "x" (zmm) : "xmm5" ); in pltenter()
188 asm volatile ("vmovdqa64 %0, %%zmm6" : : "x" (zmm) : "xmm6" ); in pltenter()
189 asm volatile ("vmovdqa64 %0, %%zmm7" : : "x" (zmm) : "xmm7" ); in pltenter()
216 __m512i zmm = _mm512_set1_epi64 (i + 1); in pltexit() local
217 if (memcmp (&inregs->lr_vector[i], &zmm, sizeof (zmm)) != 0) in pltexit()
221 outregs->lrv_vector0.zmm[0] in pltexit()
224 __m512i zmm = _mm512_set1_epi64 (-1); in pltexit() local
225 asm volatile ("vmovdqa64 %0, %%zmm0" : : "x" (zmm) : "xmm0" ); in pltexit()
226 asm volatile ("vmovdqa64 %0, %%zmm1" : : "x" (zmm) : "xmm1" ); in pltexit()