Lines Matching refs:tp0

735     uint32_t tp0, tp1, tp2, tp3, tp4, tp5, tp6, tp7;
744 "ld.wu %[tp0], %[src], 0 \n\t"
753 "st.w %[tp0], %[dst], 0 \n\t"
763 [src]"+&r"(src), [dst]"+&r"(dst), [tp0]"+&r"(tp0), [tp1]"+&r"(tp1),
775 "ld.wu %[tp0], %[src], 0 \n\t"
779 "st.w %[tp0], %[dst], 0 \n\t"
784 [src]"+&r"(src), [dst]"+&r"(dst), [tp0]"+&r"(tp0), [tp1]"+&r"(tp1),
791 "ld.wu %[tp0], %[src], 0 \n\t"
793 "st.w %[tp0], %[dst], 0 \n\t"
795 : [tp0]"+&r"(tp0), [tp1]"+&r"(tp1)
852 __m256i tp0, tp1, tp2, tp3;
878 tp0, tp1, tp2, tp3);
879 DUP2_ARG2(__lasx_xvilvl_d, tp2, tp0, tp3, tp1, tp0, tp2);
880 tp0 = __lasx_xvpermi_q(tp2, tp0, 0x20);
881 out = __lasx_xvavgr_bu(out, tp0);
896 __m256i tp0, tp1, tp2, tp3, dst0, dst1;
938 tp0, tp1, tp2, tp3);
939 DUP2_ARG2(__lasx_xvilvl_d, tp2, tp0, tp3, tp1, tp0, tp2);
940 dst0 = __lasx_xvpermi_q(tp2, tp0, 0x20);
943 tp0, tp1, tp2, tp3);
945 DUP2_ARG2(__lasx_xvilvl_d, tp2, tp0, tp3, tp1, tp0, tp2);
946 dst1 = __lasx_xvpermi_q(tp2, tp0, 0x20);
966 __m256i tp0, tp1, tp2, tp3;
983 tp0, tp1, tp2, tp3);
984 DUP2_ARG2(__lasx_xvilvl_d, tp2, tp0, tp3, tp1, tp0, tp2);
985 tp0 = __lasx_xvpermi_q(tp2, tp0, 0x20);
986 out = __lasx_xvavgr_bu(out, tp0);
1000 __m256i tp0, tp1, tp2, tp3, dst0, dst1;
1024 tp0, tp1, tp2, tp3);
1025 DUP2_ARG2(__lasx_xvilvl_d, tp2, tp0, tp3, tp1, tp0, tp2);
1026 dst0 = __lasx_xvpermi_q(tp2, tp0, 0x20);
1029 tp0, tp1, tp2, tp3);
1031 DUP2_ARG2(__lasx_xvilvl_d, tp2, tp0, tp3, tp1, tp0, tp2);
1032 dst1 = __lasx_xvpermi_q(tp2, tp0, 0x20);
1053 __m256i tp0, tp1, tp2, tp3;
1070 tp0, tp1, tp2, tp3);
1071 DUP2_ARG2(__lasx_xvilvl_d, tp2, tp0, tp3, tp1, tp0, tp2);
1072 tp0 = __lasx_xvpermi_q(tp2, tp0, 0x20);
1073 out = __lasx_xvavgr_bu(out, tp0);
1087 __m256i tp0, tp1, tp2, tp3, dst0, dst1;
1113 tp0, tp1, tp2, tp3);
1114 DUP2_ARG2(__lasx_xvilvl_d, tp2, tp0, tp3, tp1, tp0, tp2);
1115 dst0 = __lasx_xvpermi_q(tp2, tp0, 0x20);
1118 tp0, tp1, tp2, tp3);
1120 DUP2_ARG2(__lasx_xvilvl_d, tp2, tp0, tp3, tp1, tp0, tp2);
1121 dst1 = __lasx_xvpermi_q(tp2, tp0, 0x20);