• <tr id="yyy80"></tr>
  • <sup id="yyy80"></sup>
  • <tfoot id="yyy80"><noscript id="yyy80"></noscript></tfoot>
  • 99热精品在线国产_美女午夜性视频免费_国产精品国产高清国产av_av欧美777_自拍偷自拍亚洲精品老妇_亚洲熟女精品中文字幕_www日本黄色视频网_国产精品野战在线观看 ?

    基于GPU的列車衛(wèi)星定位接收機(jī)捕獲引擎設(shè)計

    2023-09-25 13:11:14黃頌巴曉輝蔡伯根姜維王劍
    關(guān)鍵詞:頻點(diǎn)線程接收機(jī)

    黃頌,巴曉輝, ,蔡伯根 , ,姜維,,王劍,

    (1.北京交通大學(xué) 電子信息工程學(xué)院,北京 100044;2.北京交通大學(xué) 智慧高鐵系統(tǒng)前沿科學(xué)中心,北京 100044;3.北京市軌道交通電磁兼容與衛(wèi)星導(dǎo)航工程技術(shù)研究中心,北京 100044;4.北京交通大學(xué) 計算機(jī)與信息技術(shù)學(xué)院,北京 100044)

    以我國北斗、美國GPS 為代表的全球衛(wèi)星導(dǎo)航系統(tǒng)(Global Navigation Satellite System,GNSS)能夠?yàn)槿蚍秶鷥?nèi)的用戶提供定位、定速和授時等服務(wù)[1]。隨著衛(wèi)星導(dǎo)航系統(tǒng)在公路、民航等交通運(yùn)輸?shù)膹V泛應(yīng)用,下一代列控系統(tǒng)提出了應(yīng)用BDS系統(tǒng)提供位置服務(wù)的需求。在鐵路建設(shè)中,通過衛(wèi)星導(dǎo)航接收機(jī)測量線路、道岔等關(guān)鍵點(diǎn)的位置坐標(biāo),生成高精度軌道數(shù)字地圖輔助車載傳感器完成列車的高精度定位[2]。在區(qū)間內(nèi),使用衛(wèi)星導(dǎo)航接收機(jī)接收衛(wèi)星信號解算列車的速度和位置,來替代依賴應(yīng)答器與軌道電路進(jìn)行定位、占用檢查的傳統(tǒng)方法,降低了區(qū)間內(nèi)軌旁設(shè)備的數(shù)量,減輕設(shè)備維護(hù)的工作量[3]。利用衛(wèi)星導(dǎo)航系統(tǒng)建立可靠的列車運(yùn)行控制系統(tǒng),保障鐵路的安全性和可維護(hù)性是新型列控系統(tǒng)建設(shè)的關(guān)鍵問題。衛(wèi)星導(dǎo)航接收機(jī)作為提供位置服務(wù)的終端設(shè)備,不同的應(yīng)用場景對其性能參數(shù)有著不同的要求。在用于列車定位過程中,WISS 等[4]結(jié)合衛(wèi)星導(dǎo)航在鐵路定位應(yīng)用領(lǐng)域的需求,歸納形成了GNSS列車定位應(yīng)用技術(shù)開發(fā)指導(dǎo)性文件,為衛(wèi)星導(dǎo)航專用接收機(jī)相關(guān)技術(shù)發(fā)展以及實(shí)用化奠定了基礎(chǔ)。自1997 年起莫斯科COMPASS 設(shè)計局與莫斯科鐵路管理局研制列車安全設(shè)備KLUB-U,利用GPS/GLONASS 導(dǎo)航接收機(jī)及車載線路地圖實(shí)現(xiàn)列車位置的精確檢測,至今為止已在俄羅斯鐵路上千列機(jī)車上安裝使用[5]。但隨著新體制衛(wèi)星信號的播發(fā),多模多頻信號之間的兼容與互操作性給接收機(jī)的設(shè)計與發(fā)展帶來了諸多挑戰(zhàn)。常規(guī)基于ASIC(Application Specific Integrated Circuits)的硬件接收機(jī)因缺乏靈活性及不可編程性,不能對功能結(jié)構(gòu)、計算處理邏輯等進(jìn)行針對性調(diào)整,限制了接收機(jī)的性能。為對用于列車定位的接收機(jī)進(jìn)行相應(yīng)調(diào)整與優(yōu)化,科研人員引入軟件接收機(jī)的思想,采用可編程的軟件化結(jié)構(gòu)完成衛(wèi)星信號的接收處理功能。軟件接收機(jī)可對應(yīng)用于列車的輔助定位算法進(jìn)行驗(yàn)證以及為虛擬應(yīng)答器實(shí)現(xiàn)以及軌道電子地圖的生成提供服務(wù),縮短項目研發(fā)周期,降低列車定位系統(tǒng)的成本。BERTRAN 等[6]分析了鐵路設(shè)備引起的電磁干擾對硬件GPS 接收機(jī)性能的影響,驗(yàn)證了低成本的軟件接收機(jī)用于列車定位方案的必要性。上官偉等[7]設(shè)計實(shí)現(xiàn)了可用于列車定位的軟件接收機(jī),但只能捕獲強(qiáng)信噪比的衛(wèi)星信號。由于鐵路沿線存在山體、建筑、遮擋物等復(fù)雜環(huán)境,此環(huán)境下衛(wèi)星信號微弱(小于30 dBHz),而普通的商用接收機(jī)則不能正確地捕獲跟蹤信號進(jìn)行定位。為此,可利用軟件接收機(jī)的靈活性、通用性等特點(diǎn),根據(jù)不同衛(wèi)星的信號體制、鐵路沿線的應(yīng)用場景設(shè)計相應(yīng)的基帶算法,實(shí)現(xiàn)開闊場景、遮擋場景下衛(wèi)星信號的捕獲。冷啟動情況下,衛(wèi)星信號的捕獲影響列車首次定位的時間,而傳統(tǒng)的軟件接收機(jī)串行實(shí)現(xiàn)的GNSS信號捕獲算法耗時長。隨著GPU 的可編程性的不斷提高,對大規(guī)模并行數(shù)據(jù)處理的計算能力已經(jīng)在云計算、人工智能等領(lǐng)域得到應(yīng)用,為軟件接收機(jī)的實(shí)時化提供了解決方案[8]。捕獲過程可在英偉達(dá)(NVIDIA)推出的CUDA(Compute Unified Device Architecture,即統(tǒng)一計算設(shè)備架構(gòu))上進(jìn)行編程開發(fā),并行處理中頻數(shù)據(jù)。針對基于GPU 并行捕獲國內(nèi)外學(xué)者已進(jìn)行一些研究,HOBIGER 等[9]首次利用GPU實(shí)現(xiàn)了GPS的并行捕獲。HUANG等[10]設(shè)計了一種基于高性能GPU 的實(shí)時軟件接收機(jī)STARx,可并行捕獲跟蹤 GPS,Galileo,GLONASS和BDS系統(tǒng)與一些區(qū)域系統(tǒng)所有頻點(diǎn)的民用信號,滿足實(shí)時性的要求。XU 等[11]設(shè)計了一款基于GPU 的實(shí)時軟件接收機(jī)NAVSDR,在9.75 MHz復(fù)采樣率、相干積分時間為10 ms下捕獲32 顆L1 C/A 信號的速度提升約為CPU 的3.3 倍。楊智博等[12]基于嵌入式Jetson TX2 平臺,在62 MHz 采樣率下利用GPU 將B3I 信號的捕獲速度提高16.83 倍。覃新賢等[13-15]基于CUDA 平臺實(shí)現(xiàn)了北斗B1I 和B3I 信號的快速捕獲。張武迅[16]利用數(shù)據(jù)和導(dǎo)頻雙通道相干組合能捕獲到-145 dBm 的B1C 信號,進(jìn)而實(shí)現(xiàn)B1I 信號的快速位同步。若B1C和B1I的信號總功率一致時,導(dǎo)頻通道的BOC(1,1)分量占B1C 總功率的29/44,只使用導(dǎo)頻進(jìn)行捕獲會損失一定的功率;若數(shù)據(jù)通道和導(dǎo)頻通道聯(lián)合捕獲,也往往忽略BOC(6,1)分量,會損失一定的信號功率;此外若沒有對子碼剝離,捕獲B1C 信號只能使用10 ms 相干積分長度。本文在上述基礎(chǔ)上,結(jié)合基于FFT 的并行碼相位捕獲算法[17],設(shè)計了基于GPU 的強(qiáng)信號與弱信號的并行捕獲架構(gòu)。在鐵路開闊場景下,利用短時間的非相干積分對強(qiáng)信號實(shí)現(xiàn)多通道的并行捕獲;在具有遮擋的條件下,采用全比特法實(shí)現(xiàn)微弱信號的捕獲。本文著重論述了GPU 架構(gòu)下并行信號捕獲的耗時以及弱信號捕獲靈敏度,提出的碼多普勒補(bǔ)償?shù)碾p模并行捕獲方法在強(qiáng)信號場景下提升捕獲的速度,在弱信號場景下提高捕獲靈敏度的同時有效減少了弱信號的捕獲耗時?;贕PU 的強(qiáng)弱信號并行捕獲架構(gòu)場景靈活度高,便于算法驗(yàn)證,可在普通的PC機(jī)上運(yùn)行,設(shè)備成本低。

    1 基于FFT的信號捕獲算法

    GPS L1 C/A 和BDS B1I 信號經(jīng)過射頻前端下變頻、采樣后得到的中頻信號分別表示如下:

    式中:j 表示衛(wèi)星的PRN 號;A 表示信號幅度;C表示擴(kuò)頻碼;D 表示擴(kuò)頻碼上面調(diào)制的導(dǎo)航電文;NH表示調(diào)制的二級碼;fIF是載波中頻頻率;fd為載波多普勒;φ0是載波初始相位。

    衛(wèi)星信號捕獲的實(shí)質(zhì)是將接收信號與本地復(fù)現(xiàn)的載波和擴(kuò)頻碼作相關(guān)運(yùn)算,得到相關(guān)峰值,根據(jù)設(shè)置的閾值進(jìn)行門限判決,從而得到衛(wèi)星PRN號、碼相位和載波多普勒估計值。GPS L1C/A與BDS 的B1I信號采用BPSK 調(diào)制方式,導(dǎo)航電文每20 ms 可能出現(xiàn)一次比特翻轉(zhuǎn),但對于MEO 和IGSO 衛(wèi)星B1I信號上還存在的1 kbps的NH 碼,可能會在相干積分時間內(nèi)出現(xiàn)二級碼翻轉(zhuǎn),導(dǎo)致相干增益的削減。本文采用補(bǔ)零FFT[18]的方法來解決B1I 信號二級碼跳變產(chǎn)生的不利影響,算法原理如圖1所示。

    圖1 信號捕獲算法示意圖Fig.1 Schematic diagram of signal acquisition algorithm

    為了消除電文翻轉(zhuǎn)或者二級碼跳變產(chǎn)生的影響,每次使用2 ms 的中頻數(shù)據(jù),這是因?yàn)? ms 至少會包含一個完整周期的擴(kuò)頻碼,但最終只保留前1 ms 有效結(jié)果。對于強(qiáng)信號捕獲只需對最終產(chǎn)生的1 ms 相關(guān)值取模進(jìn)行非相干累積得到捕獲檢測量。而對于弱信號捕獲,本文采用全比特法充分利用一個比特的相干積分時間(20 ms),需要將1 ms相關(guān)值進(jìn)行20 次相干累積,再進(jìn)行非相干累加得到最終捕獲檢測量。不同于強(qiáng)信號的是,弱信號捕獲不僅需要對不同載波頻點(diǎn)、碼相位進(jìn)行搜索,還需要搜索20 次導(dǎo)航電文的比特邊沿,并且為了減少因碼多普勒頻移造成的影響,本地復(fù)制的碼相位需根據(jù)當(dāng)前搜索的載波多普勒進(jìn)行調(diào)整。

    2 基于CPU 與GPU 的強(qiáng)弱信號捕獲架構(gòu)設(shè)計

    信號捕獲過程中的點(diǎn)乘、相干、非相干累加等都存在大量的重復(fù)性工作,且每個采樣點(diǎn)的計算都是獨(dú)立的,符合GPU 運(yùn)算單指令多數(shù)據(jù)流(Single Instruction Multiple Data,SIMD)的規(guī)則。其次,不同的衛(wèi)星在搜索每個頻點(diǎn)的處理流程也是相同的,即不同衛(wèi)星、不同搜索頻點(diǎn)之間的相關(guān)運(yùn)算是相對獨(dú)立的運(yùn)算過程,故可以采用并行計算方式來處理。英偉達(dá)公司開發(fā)的CUDA 并行計算架構(gòu)采用了單指令多線程執(zhí)行模型,可以設(shè)計合適的并行結(jié)構(gòu)加速采樣點(diǎn)的計算。

    本文設(shè)計的捕獲模塊采用了CPU 與GPU 異構(gòu)并行計算的結(jié)構(gòu),強(qiáng)弱信號并行捕獲架構(gòu)如圖2所示。捕獲模塊包括本地載波產(chǎn)生、本地擴(kuò)頻碼生成、各個多普勒頻點(diǎn)的碼相位搜索、相干與非相干累加、峰值檢測及門限判決等子模塊。其中,載波剝離、FFT 運(yùn)算、向量相乘、IFFT 運(yùn)算、向量累加取模等存在大量數(shù)據(jù)運(yùn)算的操作,可以將其交與GPU 端并行化處理,提升捕獲的速度;而CPU 端則讀取中頻數(shù)據(jù)等復(fù)雜的邏輯運(yùn)算,完成門限判決與存儲捕獲結(jié)果。

    圖2 信號并行捕獲架構(gòu)Fig.2 Signal parallel acquisition architecture

    從CPU 端讀取中頻信號采樣點(diǎn)并且生成多顆衛(wèi)星的擴(kuò)頻碼,并將中頻信號、擴(kuò)頻碼采樣點(diǎn)由CPU 內(nèi)存拷貝到GPU 顯存中進(jìn)行并行運(yùn)算,最終得到多個1 ms 有效數(shù)據(jù)。對于強(qiáng)信號捕獲進(jìn)行多次非相干積分即可,而微弱信號捕獲利用了20 ms相干積分時間,為防止相干增益被抵消需要并行搜索導(dǎo)航電文的比特邊沿。得到每個碼相位(采樣點(diǎn))的累加值后,最終在GPU 端搜索碼相位的最大峰值,將其拷貝至CPU 中進(jìn)行門限判決得到捕獲結(jié)果。綜上,強(qiáng)弱信號捕獲需具體設(shè)計相應(yīng)的核函數(shù)完成各自計算任務(wù)的并行處理。

    3 并行計算模型設(shè)計

    3.1 載波相位并行線程模型

    CUDA 是由NVIDIA 推出的專門用于GPU 編程開發(fā)的平臺,其編程模型如圖3 所示。CPU 與GPU 通過PCIe 總線相連接來協(xié)同工作,CPU 所在位置稱為為主機(jī)端(host),其包含的存儲空間稱為主機(jī)內(nèi)存;而GPU 所在位置稱為設(shè)備端(device),包含的存儲空間稱為設(shè)備內(nèi)存。CUDA 的線程組織結(jié)構(gòu)[19]如圖3 所示,自上到下可以分為Grid,Block和Thread 3級,多個線程(Thread)組成一個線程塊(Block),多個線程塊構(gòu)成一個網(wǎng)格(Grid),一個網(wǎng)格對應(yīng)著一個核函數(shù)(運(yùn)行在GPU 上的并行計算函數(shù))。在CUDA 中每一個線程都要執(zhí)行核函數(shù),所以每個線程會分配一個唯一的線程號,并且每一級都有其相應(yīng)的編號,從而利用編號使線程執(zhí)行并行計算的任務(wù)。

    圖3 CUDA線程組織架構(gòu)Fig.3 CUDA thread organization architecture

    在進(jìn)行載波剝離的過程中,本地載波相位的計算是通過數(shù)控振蕩器的形式來實(shí)現(xiàn),每次步進(jìn)的長度是由載波多普勒頻移計算得到,若在CPU以串行的方式計算中頻信號采樣點(diǎn)數(shù)值時,每個點(diǎn)的載波相位和碼相位是通過上一個采樣點(diǎn)與步進(jìn)值累加得到。本文利用GPU 對每個采樣點(diǎn)并行生成,無法依據(jù)上一個采樣點(diǎn)進(jìn)行推導(dǎo),可以根據(jù)線程編號來索引每一個采樣點(diǎn)。因此本地載波生成的并行計算模型可設(shè)計為一維Block 和二維Grid 的結(jié)構(gòu),由此可以得到每個采樣點(diǎn)的載波相位為:

    其中:threadIdx.x 為每個Block 內(nèi)線程的列編號,blockIdx.x 為Grid 中Block 的列編號,生成不同頻點(diǎn)的載波可用blockIdx.y來索引。

    3.2 碼相位并行線程模型

    本地碼相位的生成方式與載波相位相同,也是通過數(shù)控振蕩器的形式來實(shí)現(xiàn),但衛(wèi)星和接收機(jī)之間的相對運(yùn)動會產(chǎn)生碼多普勒效應(yīng),衛(wèi)星信號的擴(kuò)頻碼頻率會發(fā)生偏移,隨著時間的推移,接收信號與本地信號的碼相位將會發(fā)生相對滑動即碼相位誤差將逐漸變大,可能造成相干積分的峰值下降與移位??紤]碼多普勒的碼相位步進(jìn)長度可由式(5)表示:

    其中:frf代表衛(wèi)星射頻頻率;fcode為擴(kuò)頻碼速率;fs為采樣率。捕獲強(qiáng)信號時,使用的中頻數(shù)據(jù)短,基本可以忽略接收信號與本地信號的碼相位滑動,只需生成1 ms 長度的偽碼然后補(bǔ)1 ms 長度的0 作為本地碼。本地偽碼以并行多路的形式在GPU 生成,采用二維的Block 和一維的Thread 結(jié)構(gòu),其中Block 的X 維線程索引本地碼相位采樣點(diǎn),Y 維線程索引不同衛(wèi)星本地碼的產(chǎn)生。

    在進(jìn)行弱信號的捕獲時,需要進(jìn)行長時間的信號累積來提高靈敏度,并且載波多普勒較大時勢必造成相干積分的損失,因此需考慮碼多普勒的影響。若本地碼相位采樣點(diǎn)將根據(jù)上式計算,則需要連續(xù)生成與中頻信號相同長度的偽碼采樣點(diǎn)進(jìn)行FFT 運(yùn)算,這將占用大量的顯存資源,且進(jìn)行大點(diǎn)數(shù)的FFT 會導(dǎo)致弱信號捕獲時間大大增加。為了減少FFT 耗時、節(jié)省顯存資源,本文提出一種間隔性補(bǔ)償碼多普勒的全比特法:假設(shè)t1為接收的中頻數(shù)據(jù)的某個采樣時刻,在生成本地偽碼時,t1至t1+N(N為20 ms整數(shù)倍)時段內(nèi)Nms的偽碼采樣點(diǎn)可用從t1+N/2 時刻生成的1 ms 長度的偽碼采樣點(diǎn)替代,這樣2Nms長度的FFT運(yùn)算量減少到2 ms(補(bǔ)零后的長度),考慮到碼多普勒對碼相位滑動的影響,需要對從t1+N/2 時刻生成的1 ms 偽碼進(jìn)行碼多普勒補(bǔ)償,由此可以得到經(jīng)過碼多普勒補(bǔ)償后t1+N/2時刻開始生成的碼相位為:

    3.3 比特邊沿搜索并行線程模型

    本地偽碼采樣點(diǎn)生成后,將其FFT 結(jié)果取共軛與中頻信號的FFT 結(jié)果進(jìn)行頻域相乘,在點(diǎn)乘時采用多采樣點(diǎn)并行計算可顯著降低相關(guān)運(yùn)算的時間;對相乘的結(jié)果調(diào)用cuFFT 庫進(jìn)行IFFT 運(yùn)算,得到多個IFFT 的前1 ms 有效結(jié)果后,捕獲弱信號需要搜索比特邊沿搜索即20 次并行相干累加,設(shè)計的并行線程模型如圖4所示。

    圖4 三維并行架構(gòu)Fig.4 3D parallel architecture

    考慮到20 次相干積分中采樣點(diǎn)的相加運(yùn)算、載波頻率的搜索以及比特邊沿的搜索,并行計算模型可設(shè)計為一維的Block 和三維的Grid 的結(jié)構(gòu)。比特邊沿的搜索通過blockIdx.z 索引,不同載波頻點(diǎn)的計算則使用blockIdx.y 來索引,同時在Block內(nèi)每個線程索引1 ms 相干積分的每個采樣點(diǎn)。此外,進(jìn)行相干累加的過程中,BDS 與GPS 不同的是還需要剝離二級碼,即BDS 每1 ms 的采樣點(diǎn)都需要與NH 碼相乘才能進(jìn)行相干累加。經(jīng)過相干積分、非相干積分后的結(jié)果需要在GPU 端進(jìn)行峰值檢測,可利用CUDA的cuBLAS庫實(shí)現(xiàn)數(shù)據(jù)的并行處理,得到峰值所在的位置,最后將結(jié)果從顯存拷貝到內(nèi)存中進(jìn)行門限判決。受限于設(shè)備內(nèi)存的大小,弱信號捕獲需要處理較長的中頻數(shù)據(jù)和搜索大量的載波頻點(diǎn),不可能一次性在GPU 中進(jìn)行所有載波頻點(diǎn)的并行搜索,而強(qiáng)信號捕獲則可以一次進(jìn)行所有頻點(diǎn)的并行搜索。

    3.4 內(nèi)存分配與程序優(yōu)化設(shè)計

    在Nvidia GPU 內(nèi)部為不同的數(shù)據(jù)結(jié)構(gòu)和內(nèi)存讀取方式定義了一些特殊的內(nèi)存,如寄存器、共享內(nèi)存、紋理內(nèi)存、全局內(nèi)存、鎖頁內(nèi)存等,每種不同類型的內(nèi)存空間都有不同的作用域、生命周期和緩存行為,合理利用內(nèi)存能夠提升程序的并行效率。紋理存儲器(texture memory)是一種只讀存儲器,對數(shù)據(jù)的讀(寫)操作通過專門的texture cache(紋理緩存)進(jìn)行,速度優(yōu)于全局內(nèi)存。由于GPS 與BDS 的偽隨機(jī)序列是固定不變的,偽隨機(jī)序列存放在設(shè)備端的紋理內(nèi)存之中能夠減少偽碼在GPU與CPU之間傳輸所消耗的時間。

    頁鎖定內(nèi)存是在主機(jī)內(nèi)存中開辟一塊供GPU交換數(shù)據(jù)而不與磁盤進(jìn)行數(shù)據(jù)交換的空間,具有更高的內(nèi)存讀取速度,其傳輸效率高于被交換的可分頁內(nèi)存。在處理中頻數(shù)據(jù)之前,需要將中頻數(shù)據(jù)采樣點(diǎn)從CPU 的內(nèi)存空間提前傳輸?shù)紾PU 顯存中,當(dāng)弱信號捕獲需要較長的中頻數(shù)據(jù)或者采樣頻率較高時,采樣點(diǎn)內(nèi)存的讀取將花費(fèi)大量的時間,因此可以使用頁鎖定內(nèi)存存放采樣點(diǎn)數(shù)據(jù)。

    對于中頻信號進(jìn)行載波剝離時,載波生成模塊載波生成模塊有2種常用方式,一種是在核函數(shù)中調(diào)用sincosf 進(jìn)行單精度浮點(diǎn)三角函數(shù)計算;第二種是使用查詢表的方式得到,將提前計算好的正余弦函數(shù)表存放在紋理內(nèi)存中,每次調(diào)用時根據(jù)相位讀取相應(yīng)數(shù)值,這是一種空間換時間的方式,由于GPU 具有強(qiáng)大的浮點(diǎn)計算能力,上述2種方式所花時間相差不大。

    在上一節(jié)的并行計算模型之中,無論是碼相位和載波相位的計算,還是點(diǎn)乘、相干與非相干累加,都可以采用一個線程計算多個采樣點(diǎn)的策略提高程序的運(yùn)行速度。而CUDA 核函數(shù)運(yùn)算之前需要訪問顯存讀取數(shù)據(jù),當(dāng)滿足合并訪問時,能夠?qū)崿F(xiàn)顯存帶寬的最大化利用,提高內(nèi)核函數(shù)的執(zhí)行性能。綜上,設(shè)計核函數(shù)時讓相鄰的線程計算相鄰的點(diǎn),這樣既實(shí)現(xiàn)了合并訪問又保證了單個線程計算多采樣點(diǎn)。

    4 實(shí)驗(yàn)驗(yàn)證及數(shù)據(jù)分析

    4.1 實(shí)驗(yàn)數(shù)據(jù)及設(shè)備

    本文實(shí)驗(yàn)的硬件環(huán)境如下。

    CPU:Intel Core i7-9750H;

    GPU:NVIDIA GeForce GTX 1650,計算能力7.5,顯存8 G。

    在硬件層面,GPU 是以線程束的形式在多處理器(Streaming Multiprocessor,SM)來運(yùn)行實(shí)現(xiàn)并行計算,在每個SM 中線程束的占用率越高則說明當(dāng)前程序的并行性越高。共享內(nèi)存與寄存器的占用也是影響程序效率的重要因素,并且GPU 中的硬件資源是有限的,隨著線程數(shù)量的變化,每個線程可以使用的硬件資源也不同,這是影響線程束占用率的主要因素。實(shí)驗(yàn)所使用的GPU 硬件資源如表1所示。

    表1 GPU硬件資源Table 1 GPU hardware resource

    本文使用模擬器和2018 年7 月京沈客運(yùn)專線黑山北站—沈陽西站區(qū)間實(shí)測軌跡數(shù)據(jù)仿真生成了不同信噪比的中頻測試數(shù)據(jù),以此模擬鐵路的強(qiáng)弱信號場景來進(jìn)行捕獲。在采樣率為16.368 MHz下生成的GPS 和BDS 中頻數(shù)據(jù)頻譜圖如圖5 和圖6所示。由于捕獲衛(wèi)星信號時使用的數(shù)據(jù)在該時段內(nèi)列車的速度與衛(wèi)星的速度變化微小,可認(rèn)為載波多普勒保持不變。結(jié)合以上實(shí)驗(yàn)數(shù)據(jù),本文將從捕獲速度、正確性和捕獲靈敏度分析信號并行捕獲的性能。

    圖5 GPS中頻信號頻譜圖Fig.5 Spectrogram of GPS IF signal

    圖6 BDS中頻信號頻譜圖Fig.6 Spectrogram of BDS IF signal

    4.2 捕獲速度分析

    實(shí)時性能是衡量軟件接收機(jī)的數(shù)據(jù)計算能力的關(guān)鍵因素,對于軟件接收機(jī)來說,捕獲作為計算最大的模塊,其消耗的時間會影響到冷啟動或衛(wèi)星信號失鎖時重捕的首次定位時間,從而影響到系統(tǒng)接收的實(shí)時性,本小節(jié)對強(qiáng)弱信號環(huán)境下的捕獲速度進(jìn)行分析。

    設(shè)置GPS 和BDS 強(qiáng)信號捕獲的相干積分時間為1 ms,捕獲GPS L1C/A 與BDS B1I 采用補(bǔ)零FFT 算法,對于1 ms 的相干積分需要進(jìn)行2 ms 長度的數(shù)據(jù)運(yùn)算。根據(jù)第2節(jié)可知,捕獲模塊主要由本地載波生成及剝離,本地碼生成,F(xiàn)FT/IFFT 和非相干積分等部分組成,當(dāng)采樣率相同時上述模塊中參與運(yùn)算的采樣點(diǎn)的數(shù)量是相同的,因此2種信號捕獲各模塊的運(yùn)算量基本相同,即耗時相同。

    表2 給出了62 MHz 采樣率下,單通道以及1 ms 相干積分時間內(nèi)分別搜索1 個與21 個載波多普勒的耗時。表3 列出了不同文獻(xiàn)的GPU 捕獲耗時情況,與文獻(xiàn)[16]相比,非相干次數(shù)為1 時,搜索一顆衛(wèi)星本文消耗的時間是其50%左右;與文獻(xiàn)[10]相比,本文捕獲所消耗的時間是其75%左右,由于同等架構(gòu)下Cuda 核心的數(shù)量會與運(yùn)算速度成正比,因此與本文的加速效果相差不大。

    表2 GPS/BDS強(qiáng)信號GPU捕獲耗時Table 2 Strong signal acquisition time of GPS/BDS

    表3 捕獲耗時對比Table 3 Comparison of acquisition time

    設(shè)置相干積分時間1 ms,非相干次數(shù)20 次,圖7給出了3種采樣率下不同通道數(shù)GPU 捕獲的總耗時。采樣率為16.368 MHz 時,搜索一顆衛(wèi)星且同時搜索21個頻點(diǎn),需要24 ms左右;降低采樣率為5 MHz 時,同時搜索10 顆衛(wèi)星且每顆衛(wèi)星同時搜索21個頻點(diǎn)需要27 ms左右。

    圖7 多通道捕獲總耗時Fig.7 Total time for multi-channel acquisition

    對于弱信號捕獲可以通過3.2 所述的間隔性補(bǔ)償碼多普勒的全比特法來減少耗時。若處理100 ms的中頻數(shù)據(jù)本地將生成200 ms(補(bǔ)零)長度的偽碼采樣點(diǎn)作FFT 運(yùn)算,這會使捕獲的耗時顯著增加,因此本文用第10 ms開始的1 ms采樣點(diǎn)、第30 ms 開始的1 ms 采樣點(diǎn)、第50 ms 開始的1 ms 采樣點(diǎn)、第70 ms 開始的1 ms 采樣點(diǎn)、90 ms 開始的1 ms 采樣點(diǎn)來替代0 至20 ms,20 ms 至40 ms,40至60 ms,60 m 至80 ms,80 m 至100 ms 的20 ms偽碼采樣點(diǎn),因此每個載波頻點(diǎn)200 ms 長度的偽碼FFT 運(yùn)算量降低到了10 ms。表4 給出了采用間隔性補(bǔ)償碼多普勒和連續(xù)補(bǔ)償碼多普勒的全比特法(對每一毫秒的偽碼都進(jìn)行碼多普勒補(bǔ)償)時,2種采樣率下GPS 與BDS 弱信號捕獲的運(yùn)行耗時,并且同樣采樣率下捕獲2種弱信號參與運(yùn)算采樣點(diǎn)的數(shù)量是相同的,因此捕獲各模塊的運(yùn)算量相同。

    表4 GPS/BDS弱信號GPU捕獲耗時Table 4 Weak signal acquisition time of GPS/BDS

    當(dāng)采樣率為5 MHz 時,采用間隔性補(bǔ)償碼多普勒的全比特法搜索單顆GPS/BDS 所消耗的時間相比于連續(xù)補(bǔ)償碼多普勒的全比特法減少了111.64 ms;在16.368 MHz 搜索單顆GPS/BDS 消耗的時間減少了778.05 ms。因?yàn)椴捎瞄g隔性補(bǔ)償碼多普勒的方法從產(chǎn)生本地偽碼、補(bǔ)零、本地偽碼FFT 三方面顯著減少了捕獲耗時,且采樣率越高、使用的數(shù)據(jù)越長,減少耗時越明顯。此外,由于中頻數(shù)據(jù)過長、搜索的頻點(diǎn)數(shù)目過多和比特邊沿的搜索,無疑將占用大量的顯存資源,使得GPU的并行資源達(dá)到最大限制,因此捕獲模塊就變成串并混合的形式。

    4.3 不同信噪比的正確捕獲能力

    為驗(yàn)證不同信噪比下2種并行捕獲架構(gòu)的正確捕獲能力,仿真產(chǎn)生了不同載噪比的GPS/BDS 中頻信號測試數(shù)據(jù)。強(qiáng)星捕獲的測試數(shù)據(jù)參數(shù)設(shè)置為:采樣率16.368 MHz,中頻4.092 MHz。對20 ms長度的中頻數(shù)據(jù)進(jìn)行20次非相干積分的基礎(chǔ)上啟動多顆星、多頻點(diǎn)的并行捕獲,表5 列出了GPS和BDS不同載噪比下的捕獲結(jié)果。

    表5 GPS/BDS強(qiáng)信號捕獲結(jié)果Table 5 Acquisition results of GPS/BDS strong singal

    運(yùn)行GPU 程序?qū)⒉东@的碼相位、多普勒頻移與中頻數(shù)據(jù)的原始多普勒頻移、碼相位對比,以此來驗(yàn)證捕獲的正確性。由表4~5 可知,進(jìn)行多次獨(dú)立的捕獲實(shí)驗(yàn),對不同的衛(wèi)星設(shè)置不同且較高的載噪比,GPS 與BDS 檢測到的碼相位和多普勒頻移與原始值均在誤差范圍內(nèi),證明了強(qiáng)信號并行捕獲的正確性。當(dāng)信號強(qiáng)度減弱到33 dBHz時,僅僅是非相干積分已經(jīng)不能完成弱信號的捕獲,必須延長相干積分時間來提高信噪比。

    為了驗(yàn)證本文算法對GPS/BDS 弱信號的捕獲性能,實(shí)驗(yàn)仿真對比了間隔性補(bǔ)償碼多普勒與連續(xù)補(bǔ)償碼多普勒的全比特法在大多普勒頻偏、低載噪比下的信號檢測概率。弱信號捕獲的測試數(shù)據(jù)參數(shù)設(shè)置與表3相同,GPS和BDS設(shè)置采樣率為5 MHz;中頻頻率1.25 MHz;碼片初始值延遲666個碼片,載波多普勒頻移為4 500 Hz。圖8 和圖9分別表示GPS和BDS在不同載噪比下運(yùn)行1 000次蒙特卡洛仿真的檢測概率比較結(jié)果。仿真結(jié)果表明采用間隔補(bǔ)償碼多普勒在捕獲靈敏度上與連續(xù)補(bǔ)償碼多普勒的捕獲靈敏度相差甚微,在載噪比為25 dBHz下的GPS捕獲概率能達(dá)到90%,BDS的捕獲概率能達(dá)到80%,證明了本文算法的有效性,提高了基于GPU的弱信號捕獲的速度。

    圖8 GPS算法性能對比Fig.8 Algorithms performance comparison of GPS

    圖9 BDS算法性能對比Fig.9 Algorithms performance comparison of BDS

    根據(jù)以上總結(jié)與對比,結(jié)合信號捕獲在不同線路及運(yùn)行場景中的實(shí)際需求,基于GPU 的強(qiáng)信號捕獲顯著提升了捕獲速度,可用于開闊環(huán)境、衛(wèi)星觀測條件較好的線路區(qū)域,而基于GPU 的微弱信號方案適用于沿線部分區(qū)域信號觀測條件多變、衛(wèi)星信號存在遮擋弱信號的鐵路線路。

    5 結(jié)論

    1) 針對開闊、存在遮擋的鐵路場景,將京沈高鐵的實(shí)測軌跡數(shù)據(jù)作為依據(jù),模擬了生成不同載噪比的場景文件(中頻數(shù)據(jù)),利用設(shè)計的雙模捕獲引擎實(shí)現(xiàn)了GPS/BDS強(qiáng)弱信號捕獲。

    2) 針對傳統(tǒng)信號捕獲耗時較長的問題,引入軟件無線電的思想,設(shè)計了基于GPU 與CPU 異構(gòu)并行計算架構(gòu)的衛(wèi)星信號捕獲方法,詳細(xì)分析了信號捕獲過程的并行計算模型、GPU 內(nèi)存結(jié)構(gòu)以及捕獲耗時。針對弱信號捕獲提出一種間斷性補(bǔ)償碼多普勒的全比特法來提升捕獲速度,同時保證了弱信號的捕獲靈敏度。

    3) 由于鐵路線網(wǎng)規(guī)模龐大,沿線環(huán)境復(fù)雜,還存在無衛(wèi)星信號場景的情況,后續(xù)工作將進(jìn)一步研究偽衛(wèi)星信號的捕獲方法以及新型信號體制(BOC調(diào)制)的衛(wèi)星信號捕獲算法,設(shè)計面向鐵路應(yīng)用的衛(wèi)星/偽衛(wèi)星多系統(tǒng)軟件接收機(jī),在開闊、存在遮擋以及完全遮擋的情況下能夠給列車提供位置服務(wù),配合車載傳感器實(shí)現(xiàn)列車的無縫定位。

    猜你喜歡
    頻點(diǎn)線程接收機(jī)
    基于4G MR的大數(shù)據(jù)分析優(yōu)化EPSFB語音時延
    一種用于調(diào)幅接收機(jī)AGC的設(shè)計與實(shí)現(xiàn)
    一種面向ADS-B的RNSS/RDSS雙模接收機(jī)設(shè)計
    電子制作(2018年19期)2018-11-14 02:36:40
    淺談linux多線程協(xié)作
    數(shù)字接收機(jī)故障維修與維護(hù)
    電子制作(2016年1期)2016-11-07 08:42:41
    基于多接收機(jī)的圓周SAR欺騙干擾方法
    基于測量報告數(shù)據(jù)優(yōu)化CSFB頻點(diǎn)配置的方法
    載帶壓縮11頻點(diǎn)創(chuàng)新方案
    Linux線程實(shí)現(xiàn)技術(shù)研究
    GSM網(wǎng)絡(luò)跳躍式頻率優(yōu)化方案
    在线观看人妻少妇| 久久久久精品人妻al黑| 亚洲三区欧美一区| 国产精品亚洲av一区麻豆| 午夜老司机福利片| 在线观看免费午夜福利视频| 一本—道久久a久久精品蜜桃钙片| 多毛熟女@视频| 久久精品人人爽人人爽视色| 亚洲av电影在线观看一区二区三区| 亚洲欧洲日产国产| 人成视频在线观看免费观看| 欧美日韩成人在线一区二区| 日韩,欧美,国产一区二区三区| 日本黄色日本黄色录像| 啦啦啦 在线观看视频| 久久女婷五月综合色啪小说| 最近最新中文字幕大全免费视频| 69av精品久久久久久 | 欧美日韩一级在线毛片| 国产精品亚洲av一区麻豆| 少妇的丰满在线观看| 国产成人欧美在线观看 | 考比视频在线观看| 亚洲国产欧美日韩在线播放| tube8黄色片| 欧美精品高潮呻吟av久久| 欧美老熟妇乱子伦牲交| 人人妻人人爽人人添夜夜欢视频| 欧美日韩亚洲高清精品| 伊人久久大香线蕉亚洲五| 夜夜骑夜夜射夜夜干| 日韩大码丰满熟妇| 久久久久久久大尺度免费视频| 久久精品国产综合久久久| 日韩大码丰满熟妇| 一个人免费在线观看的高清视频 | 我的亚洲天堂| 国产成人精品无人区| 99精品欧美一区二区三区四区| 男人舔女人的私密视频| 亚洲精品第二区| 免费在线观看影片大全网站| 啦啦啦 在线观看视频| 狠狠狠狠99中文字幕| 又大又爽又粗| 制服诱惑二区| 丰满迷人的少妇在线观看| 国产精品秋霞免费鲁丝片| 日日摸夜夜添夜夜添小说| 老司机亚洲免费影院| 久久精品亚洲熟妇少妇任你| 50天的宝宝边吃奶边哭怎么回事| 一级毛片女人18水好多| 国产亚洲欧美精品永久| 我的亚洲天堂| 黄片播放在线免费| 午夜视频精品福利| 不卡一级毛片| kizo精华| 俄罗斯特黄特色一大片| 男女下面插进去视频免费观看| 国产一区二区三区av在线| 日韩大片免费观看网站| 久久精品久久久久久噜噜老黄| 黄色视频在线播放观看不卡| 久久天堂一区二区三区四区| 狂野欧美激情性xxxx| 中文欧美无线码| 免费人妻精品一区二区三区视频| 久久国产精品大桥未久av| 99精品欧美一区二区三区四区| 啦啦啦免费观看视频1| 亚洲国产成人一精品久久久| 老司机在亚洲福利影院| 久久99热这里只频精品6学生| 黄色a级毛片大全视频| 成人18禁高潮啪啪吃奶动态图| 桃花免费在线播放| 青草久久国产| 国产亚洲欧美精品永久| 国产日韩一区二区三区精品不卡| 我要看黄色一级片免费的| 亚洲国产精品成人久久小说| 亚洲精品久久午夜乱码| 美女国产高潮福利片在线看| 夜夜骑夜夜射夜夜干| 12—13女人毛片做爰片一| 十八禁高潮呻吟视频| 宅男免费午夜| 免费观看av网站的网址| 99精品久久久久人妻精品| 十分钟在线观看高清视频www| 纵有疾风起免费观看全集完整版| 老司机深夜福利视频在线观看 | 在线精品无人区一区二区三| 女人高潮潮喷娇喘18禁视频| 欧美日韩黄片免| 一本久久精品| 中文字幕高清在线视频| 汤姆久久久久久久影院中文字幕| 亚洲av电影在线进入| 黄频高清免费视频| 黑丝袜美女国产一区| 国产欧美日韩精品亚洲av| 欧美精品高潮呻吟av久久| 午夜免费成人在线视频| 国产成人系列免费观看| 久久久久久久国产电影| 国产男女内射视频| 三上悠亚av全集在线观看| 18禁观看日本| 欧美亚洲日本最大视频资源| www日本在线高清视频| 午夜激情av网站| 国产成人欧美| 高清欧美精品videossex| 亚洲一码二码三码区别大吗| 免费观看人在逋| 欧美激情 高清一区二区三区| 好男人电影高清在线观看| 欧美精品av麻豆av| 国产精品一区二区在线不卡| 成人18禁高潮啪啪吃奶动态图| 一级毛片电影观看| 欧美人与性动交α欧美软件| 大片免费播放器 马上看| 一区二区三区乱码不卡18| 国产成人欧美| av在线老鸭窝| 波多野结衣av一区二区av| 女人久久www免费人成看片| 欧美黑人欧美精品刺激| 视频区欧美日本亚洲| videosex国产| 肉色欧美久久久久久久蜜桃| 性色av乱码一区二区三区2| 国产av精品麻豆| 日韩熟女老妇一区二区性免费视频| 亚洲性夜色夜夜综合| 亚洲视频免费观看视频| 精品国产一区二区三区久久久樱花| 美女大奶头黄色视频| 欧美日韩一级在线毛片| 久久精品国产亚洲av高清一级| 青草久久国产| 国产伦人伦偷精品视频| 青春草视频在线免费观看| 91成人精品电影| h视频一区二区三区| 亚洲精品美女久久av网站| 免费在线观看完整版高清| 女人久久www免费人成看片| 日本a在线网址| 亚洲av日韩精品久久久久久密| 女性生殖器流出的白浆| 亚洲精品中文字幕在线视频| 秋霞在线观看毛片| 亚洲av成人一区二区三| 一级毛片精品| 日本av手机在线免费观看| 色婷婷久久久亚洲欧美| 热99国产精品久久久久久7| 成年人午夜在线观看视频| 自拍欧美九色日韩亚洲蝌蚪91| 两个人看的免费小视频| 黄色a级毛片大全视频| 老司机福利观看| 日韩中文字幕视频在线看片| 色播在线永久视频| 一级毛片精品| 在线 av 中文字幕| 精品福利观看| 大型av网站在线播放| 久久久久国产精品人妻一区二区| 窝窝影院91人妻| 国产在视频线精品| 亚洲国产精品成人久久小说| 国产精品国产三级国产专区5o| 999精品在线视频| 99九九在线精品视频| 激情视频va一区二区三区| 午夜福利视频在线观看免费| 亚洲人成77777在线视频| 国产精品 国内视频| 婷婷丁香在线五月| 一级毛片女人18水好多| 亚洲成人手机| 天天躁日日躁夜夜躁夜夜| 飞空精品影院首页| 日韩欧美国产一区二区入口| 国产精品影院久久| 日韩视频在线欧美| 久久精品aⅴ一区二区三区四区| 亚洲欧美色中文字幕在线| 十八禁网站网址无遮挡| 久久中文看片网| 欧美日韩亚洲综合一区二区三区_| 日韩 欧美 亚洲 中文字幕| 一级毛片女人18水好多| 午夜91福利影院| 老司机影院成人| 免费在线观看日本一区| 亚洲国产中文字幕在线视频| 国产精品一区二区免费欧美 | 亚洲avbb在线观看| 又黄又粗又硬又大视频| 久久久精品免费免费高清| 麻豆国产av国片精品| 多毛熟女@视频| 亚洲精品在线美女| 亚洲国产精品一区二区三区在线| 桃红色精品国产亚洲av| 中文字幕色久视频| 亚洲欧美精品综合一区二区三区| 好男人电影高清在线观看| 国内毛片毛片毛片毛片毛片| 成人黄色视频免费在线看| 黄片播放在线免费| 国产一级毛片在线| 色精品久久人妻99蜜桃| 中国国产av一级| 999久久久精品免费观看国产| 天堂中文最新版在线下载| 亚洲国产欧美在线一区| 国产精品99久久99久久久不卡| 中文字幕人妻丝袜一区二区| 欧美日韩福利视频一区二区| 女性被躁到高潮视频| 久久久水蜜桃国产精品网| 亚洲精品自拍成人| 一区二区三区四区激情视频| 18禁观看日本| 久久女婷五月综合色啪小说| 亚洲av电影在线观看一区二区三区| 国产一级毛片在线| 叶爱在线成人免费视频播放| 久久综合国产亚洲精品| 自线自在国产av| 免费女性裸体啪啪无遮挡网站| 国产高清国产精品国产三级| 婷婷成人精品国产| 大香蕉久久网| 欧美中文综合在线视频| 狂野欧美激情性bbbbbb| 精品少妇黑人巨大在线播放| 国产欧美日韩综合在线一区二区| 亚洲精品国产av成人精品| 国产又爽黄色视频| 日韩有码中文字幕| 人妻人人澡人人爽人人| 欧美日韩亚洲高清精品| 香蕉丝袜av| 欧美另类亚洲清纯唯美| 国产精品久久久久久精品古装| 久久精品国产亚洲av高清一级| 丰满人妻熟妇乱又伦精品不卡| 动漫黄色视频在线观看| 久久久国产精品麻豆| 桃花免费在线播放| 丰满饥渴人妻一区二区三| 精品免费久久久久久久清纯 | 午夜免费鲁丝| 不卡一级毛片| 精品乱码久久久久久99久播| 纵有疾风起免费观看全集完整版| 亚洲欧美日韩高清在线视频 | 女人爽到高潮嗷嗷叫在线视频| 在线精品无人区一区二区三| 国产精品亚洲av一区麻豆| 久久久久久久大尺度免费视频| 亚洲九九香蕉| av又黄又爽大尺度在线免费看| 午夜视频精品福利| 欧美在线一区亚洲| 欧美日韩亚洲国产一区二区在线观看 | 久久影院123| 免费在线观看影片大全网站| 永久免费av网站大全| 亚洲欧美一区二区三区久久| 男女无遮挡免费网站观看| 欧美成狂野欧美在线观看| 国产老妇伦熟女老妇高清| 国产一卡二卡三卡精品| 国产区一区二久久| 成人av一区二区三区在线看 | 国产高清国产精品国产三级| 男人添女人高潮全过程视频| 欧美日韩福利视频一区二区| 秋霞在线观看毛片| 大陆偷拍与自拍| 久久久精品94久久精品| 久久国产精品男人的天堂亚洲| 男女边摸边吃奶| 国产区一区二久久| 999久久久国产精品视频| 满18在线观看网站| 一区二区三区四区激情视频| 欧美激情 高清一区二区三区| 亚洲国产av影院在线观看| 国产精品一区二区精品视频观看| 国产精品.久久久| 国产熟女午夜一区二区三区| 色婷婷久久久亚洲欧美| 99国产精品一区二区三区| 亚洲男人天堂网一区| av超薄肉色丝袜交足视频| 不卡av一区二区三区| 欧美激情 高清一区二区三区| 天天操日日干夜夜撸| 一本—道久久a久久精品蜜桃钙片| 国产日韩欧美视频二区| 久久国产精品男人的天堂亚洲| 免费女性裸体啪啪无遮挡网站| 最新的欧美精品一区二区| 两个人免费观看高清视频| 免费高清在线观看日韩| 国产日韩欧美在线精品| 亚洲国产日韩一区二区| 亚洲激情五月婷婷啪啪| 99热网站在线观看| 国产免费一区二区三区四区乱码| 建设人人有责人人尽责人人享有的| www.999成人在线观看| 人成视频在线观看免费观看| av不卡在线播放| 亚洲,欧美精品.| 国产精品偷伦视频观看了| 在线十欧美十亚洲十日本专区| 黄色视频不卡| 夫妻午夜视频| 亚洲精品中文字幕在线视频| 在线观看免费日韩欧美大片| 老司机深夜福利视频在线观看 | 国产成人影院久久av| 免费一级毛片在线播放高清视频 | 欧美亚洲日本最大视频资源| 99国产精品一区二区蜜桃av | 一级,二级,三级黄色视频| 啦啦啦视频在线资源免费观看| 自线自在国产av| 一级,二级,三级黄色视频| 亚洲国产欧美网| av欧美777| 午夜激情久久久久久久| 99国产极品粉嫩在线观看| 人人妻人人澡人人看| 一边摸一边抽搐一进一出视频| 国产在线视频一区二区| 50天的宝宝边吃奶边哭怎么回事| 日韩电影二区| 午夜老司机福利片| 一级黄色大片毛片| 亚洲精品自拍成人| 欧美精品啪啪一区二区三区 | cao死你这个sao货| 亚洲中文日韩欧美视频| 久久久国产欧美日韩av| 最新的欧美精品一区二区| 亚洲精品第二区| 久久久久精品人妻al黑| 亚洲欧洲精品一区二区精品久久久| 国产av又大| 国产精品香港三级国产av潘金莲| 捣出白浆h1v1| 美女脱内裤让男人舔精品视频| 后天国语完整版免费观看| 91精品国产国语对白视频| 两性午夜刺激爽爽歪歪视频在线观看 | 亚洲国产精品999| 亚洲成av片中文字幕在线观看| 亚洲九九香蕉| 久久九九热精品免费| 丝袜美腿诱惑在线| 最近最新免费中文字幕在线| 国产成人免费观看mmmm| netflix在线观看网站| 男人爽女人下面视频在线观看| kizo精华| 一级片免费观看大全| 法律面前人人平等表现在哪些方面 | bbb黄色大片| 国产99久久九九免费精品| 夜夜骑夜夜射夜夜干| 精品亚洲成a人片在线观看| 中文字幕另类日韩欧美亚洲嫩草| 菩萨蛮人人尽说江南好唐韦庄| 热re99久久国产66热| av在线老鸭窝| 久久99一区二区三区| 亚洲第一欧美日韩一区二区三区 | 亚洲成av片中文字幕在线观看| 欧美精品一区二区免费开放| 脱女人内裤的视频| 少妇粗大呻吟视频| 日本精品一区二区三区蜜桃| 免费女性裸体啪啪无遮挡网站| 99热国产这里只有精品6| 99久久99久久久精品蜜桃| 亚洲欧美日韩另类电影网站| 在线观看免费视频网站a站| 国产成人影院久久av| xxxhd国产人妻xxx| 免费黄频网站在线观看国产| 国产有黄有色有爽视频| 亚洲国产av新网站| www.精华液| 欧美另类亚洲清纯唯美| 一级毛片精品| 日韩欧美一区二区三区在线观看 | 国产一区二区三区av在线| 中文字幕精品免费在线观看视频| 少妇粗大呻吟视频| 精品久久久久久久毛片微露脸 | 97精品久久久久久久久久精品| 人成视频在线观看免费观看| 日韩中文字幕欧美一区二区| 欧美人与性动交α欧美精品济南到| 每晚都被弄得嗷嗷叫到高潮| 亚洲av男天堂| 久久亚洲精品不卡| 国产日韩一区二区三区精品不卡| 国产在线免费精品| 夜夜骑夜夜射夜夜干| 永久免费av网站大全| 亚洲五月色婷婷综合| 欧美成狂野欧美在线观看| 国产欧美日韩一区二区三区在线| 最新在线观看一区二区三区| 日韩 欧美 亚洲 中文字幕| 一级毛片电影观看| 欧美老熟妇乱子伦牲交| 亚洲精品国产一区二区精华液| 韩国精品一区二区三区| 大型av网站在线播放| 少妇猛男粗大的猛烈进出视频| 91老司机精品| 一本综合久久免费| 无遮挡黄片免费观看| 亚洲五月婷婷丁香| 一区二区三区四区激情视频| 大香蕉久久网| 一级毛片电影观看| 人妻 亚洲 视频| 成人三级做爰电影| 精品亚洲成a人片在线观看| 一级片'在线观看视频| 十八禁高潮呻吟视频| 黄片大片在线免费观看| 国产成人欧美| 男人操女人黄网站| 高清欧美精品videossex| 免费女性裸体啪啪无遮挡网站| 精品国产国语对白av| 国产精品久久久av美女十八| 亚洲综合色网址| 天天躁狠狠躁夜夜躁狠狠躁| 亚洲人成电影免费在线| 亚洲专区中文字幕在线| 日本wwww免费看| 老熟女久久久| 最黄视频免费看| 水蜜桃什么品种好| 亚洲av欧美aⅴ国产| 一边摸一边做爽爽视频免费| 亚洲精华国产精华精| 国产老妇伦熟女老妇高清| 亚洲视频免费观看视频| 成人影院久久| 18禁国产床啪视频网站| 青春草亚洲视频在线观看| 另类亚洲欧美激情| 午夜成年电影在线免费观看| 免费高清在线观看视频在线观看| 亚洲自偷自拍图片 自拍| 美女大奶头黄色视频| 一边摸一边抽搐一进一出视频| 久久免费观看电影| 一级a爱视频在线免费观看| 国产精品.久久久| 国产成+人综合+亚洲专区| 精品久久久久久久毛片微露脸 | 久久久久精品国产欧美久久久 | 性高湖久久久久久久久免费观看| 国产欧美日韩综合在线一区二区| 黄色 视频免费看| av福利片在线| 欧美在线黄色| 国产成人啪精品午夜网站| 999久久久精品免费观看国产| 国产av又大| 国产成人欧美| 日本撒尿小便嘘嘘汇集6| 国产亚洲av片在线观看秒播厂| 桃花免费在线播放| 热99久久久久精品小说推荐| 伦理电影免费视频| 日本黄色日本黄色录像| 91精品伊人久久大香线蕉| 欧美变态另类bdsm刘玥| 一级毛片女人18水好多| 岛国毛片在线播放| 亚洲avbb在线观看| 1024香蕉在线观看| 久久久久久久久免费视频了| 午夜福利在线免费观看网站| 人妻人人澡人人爽人人| 国产伦理片在线播放av一区| 女人爽到高潮嗷嗷叫在线视频| 久久人妻福利社区极品人妻图片| 亚洲成人免费电影在线观看| 亚洲美女黄色视频免费看| 99国产极品粉嫩在线观看| 欧美黄色淫秽网站| 欧美在线黄色| 国产99久久九九免费精品| 国产免费现黄频在线看| 亚洲一区中文字幕在线| 日韩大码丰满熟妇| 国产精品免费视频内射| 国产极品粉嫩免费观看在线| 自线自在国产av| 中文精品一卡2卡3卡4更新| avwww免费| 日本猛色少妇xxxxx猛交久久| 免费在线观看完整版高清| 亚洲 欧美一区二区三区| av欧美777| 精品国内亚洲2022精品成人 | 精品国产乱子伦一区二区三区 | 各种免费的搞黄视频| 国产免费av片在线观看野外av| 欧美大码av| 在线观看免费视频网站a站| xxxhd国产人妻xxx| 久久精品人人爽人人爽视色| 日本av手机在线免费观看| videosex国产| 亚洲欧美清纯卡通| a在线观看视频网站| 一级a爱视频在线免费观看| 亚洲精品美女久久av网站| 色婷婷久久久亚洲欧美| 亚洲国产精品一区二区三区在线| 每晚都被弄得嗷嗷叫到高潮| 欧美日韩一级在线毛片| 超碰97精品在线观看| 免费在线观看黄色视频的| 国产精品影院久久| 中国国产av一级| 亚洲精品久久成人aⅴ小说| 最黄视频免费看| 欧美97在线视频| 婷婷丁香在线五月| 热99久久久久精品小说推荐| 咕卡用的链子| 纵有疾风起免费观看全集完整版| 每晚都被弄得嗷嗷叫到高潮| av片东京热男人的天堂| 黄色 视频免费看| 婷婷丁香在线五月| 国产免费av片在线观看野外av| 国产成人a∨麻豆精品| 天堂中文最新版在线下载| 亚洲va日本ⅴa欧美va伊人久久 | av片东京热男人的天堂| 国产野战对白在线观看| 操美女的视频在线观看| 久久亚洲国产成人精品v| 久久综合国产亚洲精品| tube8黄色片| 夫妻午夜视频| 国产精品二区激情视频| 一边摸一边抽搐一进一出视频| a在线观看视频网站| 97在线人人人人妻| 免费久久久久久久精品成人欧美视频| 男女床上黄色一级片免费看| netflix在线观看网站| 少妇裸体淫交视频免费看高清 | 欧美在线一区亚洲| 999久久久国产精品视频| 在线av久久热| 99国产精品免费福利视频| 久久 成人 亚洲| 亚洲精品中文字幕一二三四区 | 久久女婷五月综合色啪小说| 高潮久久久久久久久久久不卡| 女人高潮潮喷娇喘18禁视频| av超薄肉色丝袜交足视频| 99国产精品99久久久久| 午夜福利,免费看| 人妻久久中文字幕网| 国产精品香港三级国产av潘金莲| 桃花免费在线播放| 嫩草影视91久久| 69av精品久久久久久 | 国产亚洲av片在线观看秒播厂| 久久这里只有精品19| 日韩一区二区三区影片| 大型av网站在线播放| 夜夜骑夜夜射夜夜干| 国内毛片毛片毛片毛片毛片| 久9热在线精品视频| 亚洲三区欧美一区| 亚洲av国产av综合av卡| 中文字幕制服av| 男女高潮啪啪啪动态图| 欧美日本中文国产一区发布| 久久热在线av| 91成年电影在线观看| 精品国产国语对白av| 最近最新免费中文字幕在线| 亚洲av成人不卡在线观看播放网 | 啦啦啦视频在线资源免费观看|