Return to accel_neon.cpp CVS log

Up to [Isaki's NoNo m68k/m88k emulator] / nono / vm

Annotation of nono/vm/accel_neon.cpp, revision 1.1

1.1     ! root        1: //
        !             2: // nono
        !             3: // Copyright (C) 2024 nono project
        !             4: // Licensed under nono-license.txt
        !             5: //
        !             6: 
        !             7: //
        !             8: // NEON
        !             9: //
        !            10: 
        !            11: #include "videoctlr.h"
        !            12: #include <arm_neon.h>
        !            13: 
        !            14: // コントラスト (0-254) を適用。
        !            15: // (ちなみに _gen は 1265 usec)
        !            16: /*static*/ void
        !            17: VideoCtlrDevice::RenderContrast_neon(BitmapRGBX& dst, const BitmapRGBX& src,
        !            18:        uint32 contrast)
        !            19: {
        !            20:        // この変換は一次元配列とみなしても行える。
        !            21:        // また必ずテキスト画面全域なので端数の考慮は不要。
        !            22:        uint pxlen = src.GetWidth() * src.GetHeight();
        !            23:        const uint32 *s32 = (const uint32 *)src.GetRowPtr(0);
        !            24:        uint32 *d32 = (uint32 *)dst.GetRowPtr(0);
        !            25:        uint32 *d32end  = d32 + pxlen;
        !            26: 
        !            27:        uint8x8_t vcont = vdup_n_u8(contrast);
        !            28: 
        !            29:        for (; d32 < d32end; ) {
        !            30:                // 2ピクセルずつ処理する
        !            31:                // 614 usec
        !            32: 
        !            33:                uint8x8_t  vsrc = vld1_u8((const uint8 *)s32);
        !            34:                uint16x8_t vmul = vmull_u8(vsrc, vcont);
        !            35:                uint8x8_t  vres = vrshrn_n_u16(vmul, 8);
        !            36:                vst1_u8((uint8 *)d32, vres);
        !            37:                s32 += 2;
        !            38:                d32 += 2;
        !            39:        }
        !            40: }

This archive runs on limited infrastructure. Preserving old code on modern bandwidth. Automated agents are requested to crawl responsibly.